From 62e8c4ffa93595fb0fbc8b0d0fd8116567b7d998 Mon Sep 17 00:00:00 2001 From: "aidan.belton" Date: Thu, 17 Feb 2022 10:14:04 +0000 Subject: [PATCH 1/4] Add bf16 aspect --- SYCL/Basic/aspects.cpp | 3 +++ 1 file changed, 3 insertions(+) diff --git a/SYCL/Basic/aspects.cpp b/SYCL/Basic/aspects.cpp index 2792a77814..fabd9b0416 100644 --- a/SYCL/Basic/aspects.cpp +++ b/SYCL/Basic/aspects.cpp @@ -54,6 +54,9 @@ int main() { if (plt.has(aspect::fp64)) { std::cout << " fp64" << std::endl; } + if (plt.has(aspect::bf16)) { + std::cout << " bf16" << std::endl; + } if (plt.has(aspect::int64_base_atomics)) { std::cout << " base atomic operations" << std::endl; } From 3ffdfd1c789e7ddcac3deaee9345df51a0446592 Mon Sep 17 00:00:00 2001 From: "aidan.belton" Date: Thu, 3 Mar 2022 12:08:11 +0000 Subject: [PATCH 2/4] clang format --- SYCL/Basic/aspects.cpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/SYCL/Basic/aspects.cpp b/SYCL/Basic/aspects.cpp index fabd9b0416..9c566368cc 100644 --- a/SYCL/Basic/aspects.cpp +++ b/SYCL/Basic/aspects.cpp @@ -54,7 +54,7 @@ int main() { if (plt.has(aspect::fp64)) { std::cout << " fp64" << std::endl; } - if (plt.has(aspect::bf16)) { + if (plt.has(aspect::bf16)) { std::cout << " bf16" << std::endl; } if (plt.has(aspect::int64_base_atomics)) { From 8d0f96fd62fae6485526f43e3459bb18248cf330 Mon Sep 17 00:00:00 2001 From: "aidan.belton" Date: Mon, 16 May 2022 14:54:36 +0100 Subject: [PATCH 3/4] Update aspect name --- SYCL/Basic/aspects.cpp | 4 ++-- 1 file changed, 2 insertions(+), 2 deletions(-) diff --git a/SYCL/Basic/aspects.cpp b/SYCL/Basic/aspects.cpp index 9c566368cc..9349cd4e78 100644 --- a/SYCL/Basic/aspects.cpp +++ b/SYCL/Basic/aspects.cpp @@ -54,8 +54,8 @@ int main() { if (plt.has(aspect::fp64)) { std::cout << " fp64" << std::endl; } - if (plt.has(aspect::bf16)) { - std::cout << " bf16" << std::endl; + if (plt.has(aspect::ext_oneapi_bfloat16)) { + std::cout << " ext_oneapi_bfloat16" << std::endl; } if (plt.has(aspect::int64_base_atomics)) { std::cout << " base atomic operations" << std::endl; From f4e156199bbda4ee3258d0702e1a37346a52a2c9 Mon Sep 17 00:00:00 2001 From: "aidan.belton" Date: Tue, 24 May 2022 15:43:10 +0100 Subject: [PATCH 4/4] Enable bfloat_type_cuda test and check with aspect --- SYCL/BFloat16/bfloat16_type_cuda.cpp | 15 +++++++++++---- 1 file changed, 11 insertions(+), 4 deletions(-) diff --git a/SYCL/BFloat16/bfloat16_type_cuda.cpp b/SYCL/BFloat16/bfloat16_type_cuda.cpp index 89e46884b4..30d1f122a2 100644 --- a/SYCL/BFloat16/bfloat16_type_cuda.cpp +++ b/SYCL/BFloat16/bfloat16_type_cuda.cpp @@ -1,8 +1,6 @@ // REQUIRES: gpu, cuda // RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple -Xsycl-target-backend --cuda-gpu-arch=sm_80 %s -o %t.out -// TODO: Currently the CI does not have a sm_80 capable machine. Enable the test -// execution once it does. -// RUNx: %t.out +// RUN: %t.out //==--------- bfloat16_type_cuda.cpp - SYCL bfloat16 type test -------------==// // @@ -14,4 +12,13 @@ #include "bfloat16_type.hpp" -int main() { return run_tests(); } +int main() { + bool has_bfloat16_aspect = false; + for (const auto &plt : sycl::platform::get_platforms()) { + if (plt.has(aspect::ext_oneapi_bfloat16)) + has_bfloat16_aspect = true; + } + + if (has_bfloat16_aspect) + return run_tests(); +}