From 4c85b02940f94e9e58b487dcef0e6ad00ccbfd93 Mon Sep 17 00:00:00 2001 From: Mochalova Date: Tue, 17 Mar 2020 19:00:40 +0300 Subject: [PATCH 01/13] [SYCL] Resolve min/max conflict Adding #undef macros to resolve conflict between definitions of the min and max function in the CL/sycl.h and windows.h or another min and max define. confict type from sycl and windows.h Signed-off-by: Mochalova --- sycl/include/CL/sycl/builtins.hpp | 2 ++ sycl/include/CL/sycl/detail/generic_type_traits.hpp | 3 +++ sycl/include/CL/sycl/half_type.hpp | 2 ++ 3 files changed, 7 insertions(+) diff --git a/sycl/include/CL/sycl/builtins.hpp b/sycl/include/CL/sycl/builtins.hpp index d8f577e188b7e..796973d25e284 100644 --- a/sycl/include/CL/sycl/builtins.hpp +++ b/sycl/include/CL/sycl/builtins.hpp @@ -17,6 +17,8 @@ // TODO Decide whether to mark functions with this attribute. #define __NOEXC /*noexcept*/ +#undef min +#undef max __SYCL_INLINE_NAMESPACE(cl) { namespace sycl { #ifdef __SYCL_DEVICE_ONLY__ diff --git a/sycl/include/CL/sycl/detail/generic_type_traits.hpp b/sycl/include/CL/sycl/detail/generic_type_traits.hpp index f5e37295c8321..afed5f9968fc2 100644 --- a/sycl/include/CL/sycl/detail/generic_type_traits.hpp +++ b/sycl/include/CL/sycl/detail/generic_type_traits.hpp @@ -18,6 +18,9 @@ #include #include +#undef min +#undef max + __SYCL_INLINE_NAMESPACE(cl) { namespace sycl { namespace detail { diff --git a/sycl/include/CL/sycl/half_type.hpp b/sycl/include/CL/sycl/half_type.hpp index 647a0abff7fff..9f13b29bfee89 100644 --- a/sycl/include/CL/sycl/half_type.hpp +++ b/sycl/include/CL/sycl/half_type.hpp @@ -25,6 +25,8 @@ #else #define __SYCL_CONSTEXPR_ON_DEVICE #endif +#undef min +#undef max __SYCL_INLINE_NAMESPACE(cl) { namespace sycl { From ebbd5af38d6de13a1a9641d8a39a9351c88263f8 Mon Sep 17 00:00:00 2001 From: Mochalova Date: Fri, 20 Mar 2020 18:22:44 +0300 Subject: [PATCH 02/13] Apply comments Use adding brackets around min & max function declarations instead of macros Signed-off-by: Mochalova --- sycl/include/CL/sycl/builtins.hpp | 28 +++++++++---------- .../CL/sycl/detail/generic_type_traits.hpp | 6 ++-- sycl/include/CL/sycl/half_type.hpp | 6 ++-- 3 files changed, 17 insertions(+), 23 deletions(-) diff --git a/sycl/include/CL/sycl/builtins.hpp b/sycl/include/CL/sycl/builtins.hpp index 796973d25e284..e08c51f329a54 100644 --- a/sycl/include/CL/sycl/builtins.hpp +++ b/sycl/include/CL/sycl/builtins.hpp @@ -17,8 +17,6 @@ // TODO Decide whether to mark functions with this attribute. #define __NOEXC /*noexcept*/ -#undef min -#undef max __SYCL_INLINE_NAMESPACE(cl) { namespace sycl { #ifdef __SYCL_DEVICE_ONLY__ @@ -532,7 +530,7 @@ detail::enable_if_t::value, T> abs(T x) __NOEXC { // genfloat max (genfloat x, genfloat y) template -detail::enable_if_t::value, T> max(T x, T y) __NOEXC { +detail::enable_if_t::value, T> (max)(T x, T y) __NOEXC { return __sycl_std::__invoke_fmax_common(x, y); } @@ -541,13 +539,13 @@ detail::enable_if_t::value, T> max(T x, T y) __NOEXC { // genfloath max (genfloath x, half y) template detail::enable_if_t::value, T> -max(T x, typename T::element_type y) __NOEXC { +(max)(T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_fmax_common(x, T(y)); } // genfloat min (genfloat x, genfloat y) template -detail::enable_if_t::value, T> min(T x, T y) __NOEXC { +detail::enable_if_t::value, T> (min)(T x, T y) __NOEXC { return __sycl_std::__invoke_fmin_common(x, y); } @@ -556,7 +554,7 @@ detail::enable_if_t::value, T> min(T x, T y) __NOEXC { // genfloath min (genfloath x, half y) template detail::enable_if_t::value, T> -min(T x, typename T::element_type y) __NOEXC { +(min)(T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_fmin_common(x, T(y)); } @@ -768,60 +766,60 @@ detail::enable_if_t::value, T> mad_sat(T a, T b, // igeninteger max (igeninteger x, igeninteger y) template -detail::enable_if_t::value, T> max(T x, T y) __NOEXC { +detail::enable_if_t::value, T> (max)(T x, T y) __NOEXC { return __sycl_std::__invoke_s_max(x, y); } // ugeninteger max (ugeninteger x, ugeninteger y) template -detail::enable_if_t::value, T> max(T x, T y) __NOEXC { +detail::enable_if_t::value, T> (max)(T x, T y) __NOEXC { return __sycl_std::__invoke_u_max(x, y); } // igeninteger max (vigeninteger x, sigeninteger y) template detail::enable_if_t::value, T> -max(T x, typename T::element_type y) __NOEXC { +(max)(T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_s_max(x, T(y)); } // vugeninteger max (vugeninteger x, sugeninteger y) template detail::enable_if_t::value, T> -max(T x, typename T::element_type y) __NOEXC { +(max)(T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_u_max(x, T(y)); } // igeninteger min (igeninteger x, igeninteger y) template -detail::enable_if_t::value, T> min(T x, T y) __NOEXC { +detail::enable_if_t::value, T> (min)(T x, T y) __NOEXC { return __sycl_std::__invoke_s_min(x, y); } // ugeninteger min (ugeninteger x, ugeninteger y) template -detail::enable_if_t::value, T> min(T x, T y) __NOEXC { +detail::enable_if_t::value, T> (min)(T x, T y) __NOEXC { return __sycl_std::__invoke_u_min(x, y); } // vigeninteger min (vigeninteger x, sigeninteger y) template detail::enable_if_t::value, T> -min(T x, typename T::element_type y) __NOEXC { +(min)(T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_s_min(x, T(y)); } // vugeninteger min (vugeninteger x, sugeninteger y) template detail::enable_if_t::value, T> -min(T x, typename T::element_type y) __NOEXC { +(min)(T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_u_min(x, T(y)); } // geninteger mul_hi (geninteger x, geninteger y) template detail::enable_if_t::value, T> mul_hi(T x, - T y) __NOEXC { + T y) __NOEXC { return __sycl_std::__invoke_s_mul_hi(x, y); } diff --git a/sycl/include/CL/sycl/detail/generic_type_traits.hpp b/sycl/include/CL/sycl/detail/generic_type_traits.hpp index afed5f9968fc2..bccaee86c1a1f 100644 --- a/sycl/include/CL/sycl/detail/generic_type_traits.hpp +++ b/sycl/include/CL/sycl/detail/generic_type_traits.hpp @@ -18,8 +18,6 @@ #include #include -#undef min -#undef max __SYCL_INLINE_NAMESPACE(cl) { namespace sycl { @@ -585,11 +583,11 @@ struct RelConverter< }; template static constexpr T max_v() { - return std::numeric_limits::max(); + return (std::numeric_limits::max)(); } template static constexpr T min_v() { - return std::numeric_limits::min(); + return (std::numeric_limits::min)(); } template static constexpr T quiet_NaN() { diff --git a/sycl/include/CL/sycl/half_type.hpp b/sycl/include/CL/sycl/half_type.hpp index 9f13b29bfee89..2519e18b80243 100644 --- a/sycl/include/CL/sycl/half_type.hpp +++ b/sycl/include/CL/sycl/half_type.hpp @@ -25,8 +25,6 @@ #else #define __SYCL_CONSTEXPR_ON_DEVICE #endif -#undef min -#undef max __SYCL_INLINE_NAMESPACE(cl) { namespace sycl { @@ -308,11 +306,11 @@ template <> struct numeric_limits { static constexpr const float_round_style round_style = round_to_nearest; - static __SYCL_CONSTEXPR_ON_DEVICE const half min() noexcept { + static __SYCL_CONSTEXPR_ON_DEVICE const half (min)() noexcept { return SYCL_HLF_MIN; } - static __SYCL_CONSTEXPR_ON_DEVICE const half max() noexcept { + static __SYCL_CONSTEXPR_ON_DEVICE const half (max)() noexcept { return SYCL_HLF_MAX; } From 07841856a2190ad8b03e1686d94a148f5bca5649 Mon Sep 17 00:00:00 2001 From: amochalo Date: Mon, 23 Mar 2020 20:48:02 +0300 Subject: [PATCH 03/13] Clang-format fix Signed-off-by: amochalo --- sycl/include/CL/sycl/builtins.hpp | 37 ++++++++++--------- .../CL/sycl/detail/generic_type_traits.hpp | 1 - sycl/include/CL/sycl/half_type.hpp | 4 +- 3 files changed, 22 insertions(+), 20 deletions(-) diff --git a/sycl/include/CL/sycl/builtins.hpp b/sycl/include/CL/sycl/builtins.hpp index e08c51f329a54..02f799ca79e77 100644 --- a/sycl/include/CL/sycl/builtins.hpp +++ b/sycl/include/CL/sycl/builtins.hpp @@ -538,14 +538,14 @@ detail::enable_if_t::value, T> (max)(T x, T y) __NOEXC { // genfloatd max (genfloatd x, double y) // genfloath max (genfloath x, half y) template -detail::enable_if_t::value, T> -(max)(T x, typename T::element_type y) __NOEXC { +detail::enable_if_t::value, T>(max)( + T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_fmax_common(x, T(y)); } // genfloat min (genfloat x, genfloat y) template -detail::enable_if_t::value, T> (min)(T x, T y) __NOEXC { +detail::enable_if_t::value, T>(min)(T x, T y) __NOEXC { return __sycl_std::__invoke_fmin_common(x, y); } @@ -553,8 +553,8 @@ detail::enable_if_t::value, T> (min)(T x, T y) __NOEXC { // genfloatd min (genfloatd x, double y) // genfloath min (genfloath x, half y) template -detail::enable_if_t::value, T> -(min)(T x, typename T::element_type y) __NOEXC { +detail::enable_if_t::value, T>(min)( + T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_fmin_common(x, T(y)); } @@ -772,54 +772,57 @@ detail::enable_if_t::value, T> (max)(T x, T y) __NOEXC // ugeninteger max (ugeninteger x, ugeninteger y) template -detail::enable_if_t::value, T> (max)(T x, T y) __NOEXC { +detail::enable_if_t::value, T>(max)(T x, + T y) __NOEXC { return __sycl_std::__invoke_u_max(x, y); } // igeninteger max (vigeninteger x, sigeninteger y) template -detail::enable_if_t::value, T> -(max)(T x, typename T::element_type y) __NOEXC { +detail::enable_if_t::value, T>(max)( + T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_s_max(x, T(y)); } // vugeninteger max (vugeninteger x, sugeninteger y) template -detail::enable_if_t::value, T> -(max)(T x, typename T::element_type y) __NOEXC { +detail::enable_if_t::value, T>(max)( + T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_u_max(x, T(y)); } // igeninteger min (igeninteger x, igeninteger y) template -detail::enable_if_t::value, T> (min)(T x, T y) __NOEXC { +detail::enable_if_t::value, T>(min)(T x, + T y) __NOEXC { return __sycl_std::__invoke_s_min(x, y); } // ugeninteger min (ugeninteger x, ugeninteger y) template -detail::enable_if_t::value, T> (min)(T x, T y) __NOEXC { +detail::enable_if_t::value, T>(min)(T x, + T y) __NOEXC { return __sycl_std::__invoke_u_min(x, y); } // vigeninteger min (vigeninteger x, sigeninteger y) template -detail::enable_if_t::value, T> -(min)(T x, typename T::element_type y) __NOEXC { +detail::enable_if_t::value, T>(min)( + T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_s_min(x, T(y)); } // vugeninteger min (vugeninteger x, sugeninteger y) template -detail::enable_if_t::value, T> -(min)(T x, typename T::element_type y) __NOEXC { +detail::enable_if_t::value, T>(min)( + T x, typename T::element_type y) __NOEXC { return __sycl_std::__invoke_u_min(x, T(y)); } // geninteger mul_hi (geninteger x, geninteger y) template detail::enable_if_t::value, T> mul_hi(T x, - T y) __NOEXC { + T y) __NOEXC { return __sycl_std::__invoke_s_mul_hi(x, y); } diff --git a/sycl/include/CL/sycl/detail/generic_type_traits.hpp b/sycl/include/CL/sycl/detail/generic_type_traits.hpp index bccaee86c1a1f..78331225d20d5 100644 --- a/sycl/include/CL/sycl/detail/generic_type_traits.hpp +++ b/sycl/include/CL/sycl/detail/generic_type_traits.hpp @@ -18,7 +18,6 @@ #include #include - __SYCL_INLINE_NAMESPACE(cl) { namespace sycl { namespace detail { diff --git a/sycl/include/CL/sycl/half_type.hpp b/sycl/include/CL/sycl/half_type.hpp index 2519e18b80243..7a65197c3478b 100644 --- a/sycl/include/CL/sycl/half_type.hpp +++ b/sycl/include/CL/sycl/half_type.hpp @@ -306,11 +306,11 @@ template <> struct numeric_limits { static constexpr const float_round_style round_style = round_to_nearest; - static __SYCL_CONSTEXPR_ON_DEVICE const half (min)() noexcept { + static __SYCL_CONSTEXPR_ON_DEVICE const half(min)() noexcept { return SYCL_HLF_MIN; } - static __SYCL_CONSTEXPR_ON_DEVICE const half (max)() noexcept { + static __SYCL_CONSTEXPR_ON_DEVICE const half(max)() noexcept { return SYCL_HLF_MAX; } From c9b1695b55be468393079d341dd8741fb4dfc5ab Mon Sep 17 00:00:00 2001 From: amochalo Date: Mon, 23 Mar 2020 20:58:40 +0300 Subject: [PATCH 04/13] Clang-format fix Signed-off-by: amochalo --- sycl/include/CL/sycl/builtins.hpp | 5 +++-- 1 file changed, 3 insertions(+), 2 deletions(-) diff --git a/sycl/include/CL/sycl/builtins.hpp b/sycl/include/CL/sycl/builtins.hpp index 02f799ca79e77..400fd080cef1f 100644 --- a/sycl/include/CL/sycl/builtins.hpp +++ b/sycl/include/CL/sycl/builtins.hpp @@ -530,7 +530,7 @@ detail::enable_if_t::value, T> abs(T x) __NOEXC { // genfloat max (genfloat x, genfloat y) template -detail::enable_if_t::value, T> (max)(T x, T y) __NOEXC { +detail::enable_if_t::value, T>(max)(T x, T y) __NOEXC { return __sycl_std::__invoke_fmax_common(x, y); } @@ -766,7 +766,8 @@ detail::enable_if_t::value, T> mad_sat(T a, T b, // igeninteger max (igeninteger x, igeninteger y) template -detail::enable_if_t::value, T> (max)(T x, T y) __NOEXC { +detail::enable_if_t::value, T>(max)(T x, + T y) __NOEXC { return __sycl_std::__invoke_s_max(x, y); } From 1218f683b9c4a6c2f2f9a024bcb1325312fa1705 Mon Sep 17 00:00:00 2001 From: Mochalova Date: Tue, 24 Mar 2020 13:38:21 +0300 Subject: [PATCH 05/13] Add test Signed-off-by: Mochalova --- sycl/test/basic_tests/min_max_test.cpp | 9 +++++++++ 1 file changed, 9 insertions(+) create mode 100644 sycl/test/basic_tests/min_max_test.cpp diff --git a/sycl/test/basic_tests/min_max_test.cpp b/sycl/test/basic_tests/min_max_test.cpp new file mode 100644 index 0000000000000..3b0c64c3d0ee9 --- /dev/null +++ b/sycl/test/basic_tests/min_max_test.cpp @@ -0,0 +1,9 @@ +#include "windows.h" +#include "CL/sycl.hpp" + +int main() { + +sycl::device device{ sycl::default_selector()}; +int tmp = min(1,4); +return 0;} + From 0d48a6b0f1400711333d71dfbc3b91ca4a76d2ab Mon Sep 17 00:00:00 2001 From: amochalo Date: Tue, 24 Mar 2020 13:47:36 +0300 Subject: [PATCH 06/13] Clang-format fix for test Signed-off-by: amochalo --- sycl/test/basic_tests/min_max_test.cpp | 8 ++++---- 1 file changed, 4 insertions(+), 4 deletions(-) diff --git a/sycl/test/basic_tests/min_max_test.cpp b/sycl/test/basic_tests/min_max_test.cpp index 3b0c64c3d0ee9..dfadf910eb273 100644 --- a/sycl/test/basic_tests/min_max_test.cpp +++ b/sycl/test/basic_tests/min_max_test.cpp @@ -3,7 +3,7 @@ int main() { -sycl::device device{ sycl::default_selector()}; -int tmp = min(1,4); -return 0;} - + sycl::device device{sycl::default_selector()}; + int tmp = min(1, 4); + return 0; +} From 3010f937c268ec3e49b425e88388fd99fc5186b8 Mon Sep 17 00:00:00 2001 From: Mochalova Date: Tue, 24 Mar 2020 16:51:05 +0300 Subject: [PATCH 07/13] Apply comments Signed-off-by: Mochalova --- sycl/test/basic_tests/min_max_test.cpp | 3 +++ 1 file changed, 3 insertions(+) diff --git a/sycl/test/basic_tests/min_max_test.cpp b/sycl/test/basic_tests/min_max_test.cpp index dfadf910eb273..c4c3c920f99c5 100644 --- a/sycl/test/basic_tests/min_max_test.cpp +++ b/sycl/test/basic_tests/min_max_test.cpp @@ -1,3 +1,6 @@ +// REQUIRES: windows +// RUN: %clangxx -fsycl %s -o %t.out + #include "windows.h" #include "CL/sycl.hpp" From cd9995e90a647a810623a8069bd3642bc79698d6 Mon Sep 17 00:00:00 2001 From: Mochalova Date: Wed, 25 Mar 2020 13:36:28 +0300 Subject: [PATCH 08/13] Apply comment Signed-off-by: Mochalova --- sycl/test/basic_tests/min_max_test.cpp | 5 ++--- 1 file changed, 2 insertions(+), 3 deletions(-) diff --git a/sycl/test/basic_tests/min_max_test.cpp b/sycl/test/basic_tests/min_max_test.cpp index c4c3c920f99c5..4546e60a306f8 100644 --- a/sycl/test/basic_tests/min_max_test.cpp +++ b/sycl/test/basic_tests/min_max_test.cpp @@ -1,12 +1,11 @@ // REQUIRES: windows -// RUN: %clangxx -fsycl %s -o %t.out +// RUN: %clangxx -fsyntax-only -Xclang -verify %s -I %sycl_include -Xclang +// expected-no-diagnostics #include "windows.h" #include "CL/sycl.hpp" int main() { - - sycl::device device{sycl::default_selector()}; int tmp = min(1, 4); return 0; } From 1fd63654e7d7c597eec850b615f76cebd475821c Mon Sep 17 00:00:00 2001 From: Mochalova Anastasiya Date: Wed, 25 Mar 2020 14:58:39 +0300 Subject: [PATCH 09/13] Update sycl/test/basic_tests/min_max_test.cpp Signed-off-by: Mochalova Co-Authored-By: Alexey Bader --- sycl/test/basic_tests/min_max_test.cpp | 1 + 1 file changed, 1 insertion(+) diff --git a/sycl/test/basic_tests/min_max_test.cpp b/sycl/test/basic_tests/min_max_test.cpp index 4546e60a306f8..5d1c54ce9ed54 100644 --- a/sycl/test/basic_tests/min_max_test.cpp +++ b/sycl/test/basic_tests/min_max_test.cpp @@ -3,6 +3,7 @@ // expected-no-diagnostics #include "windows.h" + #include "CL/sycl.hpp" int main() { From 715a22e46fccdbbc7d913addb0e5fbfe805441ad Mon Sep 17 00:00:00 2001 From: Mochalova Date: Tue, 31 Mar 2020 15:44:58 +0300 Subject: [PATCH 10/13] Apply suggestion Signed-off-by: Mochalova --- sycl/test/basic_tests/min_max_test.cpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/sycl/test/basic_tests/min_max_test.cpp b/sycl/test/basic_tests/min_max_test.cpp index 5d1c54ce9ed54..50d205eff5f5c 100644 --- a/sycl/test/basic_tests/min_max_test.cpp +++ b/sycl/test/basic_tests/min_max_test.cpp @@ -1,5 +1,5 @@ // REQUIRES: windows -// RUN: %clangxx -fsyntax-only -Xclang -verify %s -I %sycl_include -Xclang +// RUN: %clangxx -fsyntax-only -Xclang -verify %s -I %sycl_include // expected-no-diagnostics #include "windows.h" From 8089ee0ec72a33d450c0ac667e653fc4e566afa3 Mon Sep 17 00:00:00 2001 From: Mochalova Date: Tue, 31 Mar 2020 21:44:21 +0300 Subject: [PATCH 11/13] Apply comment Signed-off-by: Mochalova --- sycl/include/CL/sycl/intel/group_algorithm.hpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/sycl/include/CL/sycl/intel/group_algorithm.hpp b/sycl/include/CL/sycl/intel/group_algorithm.hpp index f4b59a2b4068e..8da599d73573d 100644 --- a/sycl/include/CL/sycl/intel/group_algorithm.hpp +++ b/sycl/include/CL/sycl/intel/group_algorithm.hpp @@ -98,7 +98,7 @@ template struct identity> { }; template struct identity> { - static constexpr T value = std::numeric_limits::max(); + static constexpr T value = (std::numeric_limits::max)(); }; template struct identity> { From 38be324962359baa45cff04db28698c3862a6e05 Mon Sep 17 00:00:00 2001 From: Mochalova Date: Wed, 1 Apr 2020 13:59:35 +0300 Subject: [PATCH 12/13] Apply comment Signed-off-by: Mochalova --- sycl/test/basic_tests/min_max_test.cpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/sycl/test/basic_tests/min_max_test.cpp b/sycl/test/basic_tests/min_max_test.cpp index 50d205eff5f5c..875a0c68882e0 100644 --- a/sycl/test/basic_tests/min_max_test.cpp +++ b/sycl/test/basic_tests/min_max_test.cpp @@ -1,5 +1,5 @@ // REQUIRES: windows -// RUN: %clangxx -fsyntax-only -Xclang -verify %s -I %sycl_include +// RUN: %clangxx -fsycl -fsycl-device-only -Xclang -verify %s -I %sycl_include // expected-no-diagnostics #include "windows.h" From 2eba9810a24a7f662b32cd0c7055ec5a1c4e8f75 Mon Sep 17 00:00:00 2001 From: Mochalova Date: Wed, 1 Apr 2020 14:12:59 +0300 Subject: [PATCH 13/13] Apply comment Signed-off-by: Mochalova --- sycl/test/basic_tests/min_max_test.cpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/sycl/test/basic_tests/min_max_test.cpp b/sycl/test/basic_tests/min_max_test.cpp index 875a0c68882e0..5934d2975846e 100644 --- a/sycl/test/basic_tests/min_max_test.cpp +++ b/sycl/test/basic_tests/min_max_test.cpp @@ -1,5 +1,5 @@ // REQUIRES: windows -// RUN: %clangxx -fsycl -fsycl-device-only -Xclang -verify %s -I %sycl_include +// RUN: %clangxx -fsycl -fsycl-device-only -fsyntax-only -Xclang -verify %s -I %sycl_include // expected-no-diagnostics #include "windows.h"