[SYCL] Fix failures on tests that use double datatype

Author: aelovikov-intel

SYCL/ESIMD/regression/dgetrf.cpp

@@ -6,7 +6,7 @@
 //
 //===----------------------------------------------------------------------===//
 
-// REQUIRES: gpu
+// REQUIRES: gpu, aspect-fp64
 // UNSUPPORTED: cuda || hip
 // RUN: %clangxx -fsycl %s -I%S/.. -o %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out 3 2 1

SYCL/ESIMD/regression/dgetrf_8x8.cpp

@@ -5,7 +5,7 @@
 // SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
 //
 //===----------------------------------------------------------------------===//
-// REQUIRES: gpu
+// REQUIRES: gpu, aspect-fp64
 // UNSUPPORTED: cuda || hip
 // RUN: %clangxx -fsycl %s -I%S/.. -o %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out 1

SYCL/ESIMD/regression/dgetrf_ref.cpp

@@ -6,7 +6,7 @@
 //
 //===----------------------------------------------------------------------===//
 
-// REQUIRES: gpu
+// REQUIRES: gpu, aspect-fp64
 // UNSUPPORTED: cuda || hip
 // RUN: %clangxx -fsycl -DUSE_REF %s -I%S/.. -o %t.ref.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.ref.out 3 2 1

SYCL/ESIMD/spec_const/spec_const_double.cpp

@@ -5,7 +5,7 @@
 // SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
 //
 //===----------------------------------------------------------------------===//
-// REQUIRES: gpu
+// REQUIRES: gpu, aspect-fp64
 // RUN: %clangxx -fsycl -I%S/.. %s -o %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out
 // UNSUPPORTED: cuda || hip

SYCL/KernelParams/union_kernel_param.cpp

@@ -12,27 +12,27 @@ union TestUnion {
 public:
   int myint;
   char mychar;
-  double mydouble;
+  float myfloat;
 
-  TestUnion() { mydouble = 0.0; };
+  TestUnion() { myfloat = 0.0f; };
 };
 
 int main(int argc, char **argv) {
   TestUnion x;
-  x.mydouble = 5.0;
-  double mydouble = 0.0;
+  x.myfloat = 5.0f;
+  float myfloat = 0.0f;
 
   sycl::queue queue;
   {
-    sycl::buffer<double, 1> buf(&mydouble, 1);
+    sycl::buffer<float, 1> buf(&myfloat, 1);
     queue.submit([&](sycl::handler &cgh) {
       auto acc = buf.get_access<sycl::access::mode::read_write>(cgh);
-      cgh.single_task<class test>([=]() { acc[0] = x.mydouble; });
+      cgh.single_task<class test>([=]() { acc[0] = x.myfloat; });
     });
   }
 
-  if (mydouble != 5.0) {
-    printf("FAILED\nmydouble = %d\n", mydouble);
+  if (myfloat != 5.0f) {
+    printf("FAILED\nmyfloat = %d\n", myfloat);
     return 1;
   }
   return 0;

SYCL/SubGroup/info.cpp

@@ -24,7 +24,7 @@ int main() {
 
   /* Basic sub-group functionality is supported as part of cl_khr_subgroups
    * extension or as core OpenCL 2.1 feature. */
-  if (!core_sg_supported(Device)) {
+  if (!core_sg_supported(Device) || !Device.has(aspect::fp64)) {
     std::cout << "Skipping test\n";
     return 0;
   }