[SYCL] Fix GCC/Clang ABI incompatibility

Resolve a regression after changing SYCL vec class to trivially copyable
that introduces ABI incompatibility between SYCL library(compiled by
GCC) and SYCL user code(compiled by CLANG) for SYCL builtin functions.
This patch resolved it by making SYCL vec class trivially copyable only
on the device side(workaround), will be fixed after detailed analysis.

Signed-off-by: Vladimir Lazarev <[email protected]>
Signed-off-by: Alexey Voronov <[email protected]>

Author: alexeyvoronov-intel

sycl/include/CL/sycl/types.hpp

@@ -350,7 +350,13 @@ template <typename Type, int NumElements> class vec {
 
   vec() { m_Data = {0}; }
 
+  // TODO Remove this difference between host and device side after
+  // when root cause of API incompatibility will be fixed
+#ifdef __SYCL_DEVICE_ONLY__
   vec(const vec &Rhs) = default;
+#else
+  vec(const vec &Rhs) : m_Data(Rhs.m_Data) {}
+#endif
 
   vec(vec &&Rhs) = default;
 

sycl/test/basic_tests/valid_kernel_args.cpp

@@ -29,6 +29,8 @@ struct SomeStructure {
   static_assert(std::is_trivially_copyable<Type>::value,                       \
                 "Is not trivially copyable type.");
 
+#ifdef __SYCL_DEVICE_ONLY__
 CHECK_PASSING_TO_KERNEL_BY_VALUE(int)
 CHECK_PASSING_TO_KERNEL_BY_VALUE(cl::sycl::cl_uchar4)
 CHECK_PASSING_TO_KERNEL_BY_VALUE(SomeStructure)
+#endif

sycl/test/built-ins/vector_common.cpp

@@ -1,4 +1,5 @@
 // RUN: %clang -std=c++11 -fsycl %s -o %t.out -lstdc++ -lOpenCL -lsycl
+// RUN: env SYCL_DEVICE_TYPE=HOST %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out
 // RUN: %ACC_RUN_PLACEHOLDER %t.out

sycl/test/built-ins/vector_geometric.cpp

@@ -1,4 +1,5 @@
 // RUN: %clang -std=c++11 -fsycl %s -o %t.out -lstdc++ -lOpenCL -lsycl
+// RUN: env SYCL_DEVICE_TYPE=HOST %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out
 // RUN: %ACC_RUN_PLACEHOLDER %t.out

sycl/test/built-ins/vector_integer.cpp

@@ -1,4 +1,5 @@
 // RUN: %clang -std=c++11 -fsycl %s -o %t.out -lstdc++ -lOpenCL -lsycl
+// RUN: env SYCL_DEVICE_TYPE=HOST %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out
 // RUN: %ACC_RUN_PLACEHOLDER %t.out

sycl/test/built-ins/vector_math.cpp

@@ -1,4 +1,5 @@
 // RUN: %clang -std=c++11 -fsycl %s -o %t.out -lstdc++ -lOpenCL -lsycl
+// RUN: env SYCL_DEVICE_TYPE=HOST %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out
 // RUN: %ACC_RUN_PLACEHOLDER %t.out

sycl/test/built-ins/vector_relational.cpp

@@ -1,4 +1,5 @@
 // RUN: %clang -std=c++11 -fsycl %s -o %t.out -lstdc++ -lOpenCL -lsycl
+// RUN: env SYCL_DEVICE_TYPE=HOST %t.out
 // RUN: %CPU_RUN_PLACEHOLDER %t.out
 // RUN: %GPU_RUN_PLACEHOLDER %t.out
 // RUN: %ACC_RUN_PLACEHOLDER %t.out