check SYCL_EXT_ONEAPI_COMPLEX_ALGORITHMS and aspect::fp64

Signed-off-by: Chris Perkins <[email protected]>

Author: cperkinsintel

SYCL/GroupAlgorithm/exclusive_scan_sycl2020.cpp

@@ -190,6 +190,7 @@ int main() {
   // https://github.com/intel/llvm/pull/5108/ ) joint_exclusive_scan and
   // exclusive_scan_over_group now operate on std::complex limited to using the
   // sycl::plus binary operation.
+#ifdef SYCL_EXT_ONEAPI_COMPLEX_ALGORITHMS
   std::array<std::complex<float>, N> input_cf;
   std::array<std::complex<float>, N> output_cf;
   std::iota(input_cf.begin(), input_cf.end(), 0);
@@ -198,13 +199,22 @@ int main() {
                                      sycl::plus<std::complex<float>>(), 0);
   test<class KernelNamePlusUnspecF>(q, input_cf, output_cf, sycl::plus<>(), 0);
 
-  std::array<std::complex<double>, N> input_cd;
-  std::array<std::complex<double>, N> output_cd;
-  std::iota(input_cd.begin(), input_cd.end(), 0);
-  std::fill(output_cd.begin(), output_cd.end(), 0);
-  test<class KernelNamePlusComplexD>(q, input_cd, output_cd,
-                                     sycl::plus<std::complex<double>>(), 0);
-  test<class KernelNamePlusUnspecD>(q, input_cd, output_cd, sycl::plus<>(), 0);
+  if (q.get_device().has(aspect::fp64)) {
+    std::array<std::complex<double>, N> input_cd;
+    std::array<std::complex<double>, N> output_cd;
+    std::iota(input_cd.begin(), input_cd.end(), 0);
+    std::fill(output_cd.begin(), output_cd.end(), 0);
+    test<class KernelNamePlusComplexD>(q, input_cd, output_cd,
+                                       sycl::plus<std::complex<double>>(), 0);
+    test<class KernelNamePlusUnspecD>(q, input_cd, output_cd, sycl::plus<>(),
+                                      0);
+  } else {
+    std::cout << "aspect::fp64 not supported. skipping std::complex<double>"
+              << std::endl;
+  }
+#else
+  static_assert(false, "SYCL_EXT_ONEAPI_COMPLEX_ALGORITHMS not defined");
+#endif
 
   std::cout << "Test passed." << std::endl;
 }

SYCL/GroupAlgorithm/inclusive_scan_sycl2020.cpp

@@ -190,6 +190,7 @@ int main() {
   // https://github.com/intel/llvm/pull/5108/ ) joint_inclusive_scan and
   // inclusive_scan_over_group now operate on std::complex limited to using the
   // sycl::plus binary operation.
+#ifdef SYCL_EXT_ONEAPI_COMPLEX_ALGORITHMS
   std::array<std::complex<float>, N> input_cf;
   std::array<std::complex<float>, N> output_cf;
   std::iota(input_cf.begin(), input_cf.end(), 0);
@@ -198,13 +199,21 @@ int main() {
                                      sycl::plus<std::complex<float>>(), 0);
   test<class KernelNamePlusUnspecF>(q, input_cf, output_cf, sycl::plus<>(), 0);
 
-  std::array<std::complex<double>, N> input_cd;
-  std::array<std::complex<double>, N> output_cd;
-  std::iota(input_cd.begin(), input_cd.end(), 0);
-  std::fill(output_cd.begin(), output_cd.end(), 0);
-  test<class KernelNamePlusComplexD>(q, input_cd, output_cd,
-                                     sycl::plus<std::complex<double>>(), 0);
-  test<class KernelNamePlusUnspecD>(q, input_cd, output_cd, sycl::plus<>(), 0);
-
+  if (q.get_device().has(aspect::fp64)) {
+    std::array<std::complex<double>, N> input_cd;
+    std::array<std::complex<double>, N> output_cd;
+    std::iota(input_cd.begin(), input_cd.end(), 0);
+    std::fill(output_cd.begin(), output_cd.end(), 0);
+    test<class KernelNamePlusComplexD>(q, input_cd, output_cd,
+                                       sycl::plus<std::complex<double>>(), 0);
+    test<class KernelNamePlusUnspecD>(q, input_cd, output_cd, sycl::plus<>(),
+                                      0);
+  } else {
+    std::cout << "aspect::fp64 not supported. skipping std::complex<double>"
+              << std::endl;
+  }
+#else
+  static_assert(false, "SYCL_EXT_ONEAPI_COMPLEX_ALGORITHMS not defined");
+#endif
   std::cout << "Test passed." << std::endl;
 }

SYCL/GroupAlgorithm/reduce_sycl2020.cpp

@@ -94,6 +94,7 @@ int main() {
   // https://github.com/intel/llvm/pull/5108/ ) joint_reduce and
   // reduce_over_group now operate on std::complex limited to using the
   // sycl::plus binary operation.
+#ifdef SYCL_EXT_ONEAPI_COMPLEX_ALGORITHMS
   std::array<std::complex<float>, N> input_cf;
   std::array<std::complex<float>, 4> output_cf;
   std::iota(input_cf.begin(), input_cf.end(), 0);
@@ -102,13 +103,22 @@ int main() {
                                      sycl::plus<std::complex<float>>(), 0);
   test<class KernelNamePlusUnspecF>(q, input_cf, output_cf, sycl::plus<>(), 0);
 
-  std::array<std::complex<double>, N> input_cd;
-  std::array<std::complex<double>, 4> output_cd;
-  std::iota(input_cd.begin(), input_cd.end(), 0);
-  std::fill(output_cd.begin(), output_cd.end(), 0);
-  test<class KernelNamePlusComplexD>(q, input_cd, output_cd,
-                                     sycl::plus<std::complex<double>>(), 0);
-  test<class KernelNamePlusUnspecD>(q, input_cd, output_cd, sycl::plus<>(), 0);
+  if (q.get_device().has(aspect::fp64)) {
+    std::array<std::complex<double>, N> input_cd;
+    std::array<std::complex<double>, 4> output_cd;
+    std::iota(input_cd.begin(), input_cd.end(), 0);
+    std::fill(output_cd.begin(), output_cd.end(), 0);
+    test<class KernelNamePlusComplexD>(q, input_cd, output_cd,
+                                       sycl::plus<std::complex<double>>(), 0);
+    test<class KernelNamePlusUnspecD>(q, input_cd, output_cd, sycl::plus<>(),
+                                      0);
+  } else {
+    std::cout << "aspect::fp64 not supported. skipping std::complex<double>"
+              << std::endl;
+  }
+#else
+  static_assert(false, "SYCL_EXT_ONEAPI_COMPLEX_ALGORITHMS not defined");
+#endif
 
   std::cout << "Test passed." << std::endl;
 }