diff --git a/libdevice/cmake/modules/SYCLLibdevice.cmake b/libdevice/cmake/modules/SYCLLibdevice.cmake index 080e2e575e540..022f5e077cb03 100644 --- a/libdevice/cmake/modules/SYCLLibdevice.cmake +++ b/libdevice/cmake/modules/SYCLLibdevice.cmake @@ -32,6 +32,15 @@ set(compile_opts -sycl-std=2020 ) +if (CMAKE_CXX_COMPILER_ID STREQUAL "GNU") + # If we use non-system GCC, need to pass its location when using + # freshly built clang. The system one might be very old. + get_filename_component(gcc_bin_dir ${CMAKE_CXX_COMPILER} DIRECTORY) + get_filename_component(gcc_install_dir ${gcc_bin_dir} DIRECTORY) + list(APPEND compile_opts + "--gcc-toolchain=${gcc_install_dir}") +endif() + if ("NVPTX" IN_LIST LLVM_TARGETS_TO_BUILD) string(APPEND sycl_targets_opt ",nvptx64-nvidia-cuda") list(APPEND compile_opts diff --git a/sycl/include/CL/__spirv/spirv_ops.hpp b/sycl/include/CL/__spirv/spirv_ops.hpp index 7eaa886c74328..a25e4cec28c95 100644 --- a/sycl/include/CL/__spirv/spirv_ops.hpp +++ b/sycl/include/CL/__spirv/spirv_ops.hpp @@ -338,7 +338,7 @@ extern SYCL_EXTERNAL TempRetT __spirv_ImageSampleExplicitLod(SampledType, // of atomic min/max based on the type #define __SPIRV_ATOMIC_MINMAX(AS, Op) \ template \ - typename sycl::detail::enable_if_t< \ + typename std::enable_if_t< \ std::is_integral::value && std::is_signed::value, T> \ __spirv_Atomic##Op(AS T *Ptr, __spv::Scope::Flag Memory, \ __spv::MemorySemanticsMask::Flag Semantics, \ @@ -346,7 +346,7 @@ extern SYCL_EXTERNAL TempRetT __spirv_ImageSampleExplicitLod(SampledType, return __spirv_AtomicS##Op(Ptr, Memory, Semantics, Value); \ } \ template \ - typename sycl::detail::enable_if_t< \ + typename std::enable_if_t< \ std::is_integral::value && !std::is_signed::value, T> \ __spirv_Atomic##Op(AS T *Ptr, __spv::Scope::Flag Memory, \ __spv::MemorySemanticsMask::Flag Semantics, \ @@ -354,7 +354,7 @@ extern SYCL_EXTERNAL TempRetT __spirv_ImageSampleExplicitLod(SampledType, return __spirv_AtomicU##Op(Ptr, Memory, Semantics, Value); \ } \ template \ - typename sycl::detail::enable_if_t::value, T> \ + typename std::enable_if_t::value, T> \ __spirv_Atomic##Op(AS T *Ptr, __spv::Scope::Flag Memory, \ __spv::MemorySemanticsMask::Flag Semantics, \ T Value) { \ diff --git a/sycl/include/sycl/accessor.hpp b/sycl/include/sycl/accessor.hpp index 42a2c262b5b17..95bb33aa71554 100644 --- a/sycl/include/sycl/accessor.hpp +++ b/sycl/include/sycl/accessor.hpp @@ -346,30 +346,28 @@ class accessor_common { MIDs[0] = Index; } - template 1)>> + template 1)>> auto operator[](size_t Index) { MIDs[Dims - CurDims] = Index; return AccessorSubscript(MAccessor, MIDs); } template > + typename = std::enable_if_t> RefType operator[](size_t Index) const { MIDs[Dims - CurDims] = Index; return MAccessor[MIDs]; } template - typename detail::enable_if_t> + typename std::enable_if_t> operator[](size_t Index) const { MIDs[Dims - CurDims] = Index; return MAccessor[MIDs]; } template > + typename = std::enable_if_t> ConstRefType operator[](size_t Index) const { MIDs[Dims - SubDims] = Index; return MAccessor[MIDs]; @@ -700,7 +698,7 @@ class image_accessor // accessor(image &imageRef); template < typename AllocatorT, int Dims = Dimensions, - typename = detail::enable_if_t<(Dims > 0 && Dims <= 3) && IsHostImageAcc>> + typename = std::enable_if_t<(Dims > 0 && Dims <= 3) && IsHostImageAcc>> image_accessor(image &ImageRef, int ImageElementSize) #ifdef __SYCL_DEVICE_ONLY__ { @@ -726,9 +724,8 @@ class image_accessor // template // accessor(image &imageRef, // handler &commandGroupHandlerRef); - template < - typename AllocatorT, int Dims = Dimensions, - typename = detail::enable_if_t<(Dims > 0 && Dims <= 3) && IsImageAcc>> + template 0 && Dims <= 3) && IsImageAcc>> image_accessor(image &ImageRef, handler &CommandGroupHandlerRef, int ImageElementSize) #ifdef __SYCL_DEVICE_ONLY__ @@ -782,17 +779,17 @@ class image_accessor size_t get_count() const { return size(); } size_t size() const noexcept { return get_range().size(); } - template > + template > range<1> get_range() const { cl_int Range = getRangeInternal(); return range<1>(Range); } - template > + template > range<2> get_range() const { cl_int2 Range = getRangeInternal(); return range<2>(Range[0], Range[1]); } - template > + template > range<3> get_range() const { cl_int3 Range = getRangeInternal(); return range<3>(Range[0], Range[1], Range[2]); @@ -803,7 +800,7 @@ class image_accessor size_t get_count() const { return size(); }; size_t size() const noexcept { return MImageCount; }; - template 0)>> + template 0)>> range get_range() const { return detail::convertToArrayOfN(getAccessRange()); } @@ -815,7 +812,7 @@ class image_accessor // || (accessTarget == access::target::host_image && ( accessMode == // access::mode::read || accessMode == access::mode::read_write)) template 0) && (IsValidCoordDataT::value) && (detail::is_genint::value) && ((IsImageAcc && IsImageAccessReadOnly) || @@ -835,7 +832,7 @@ class image_accessor // || (accessTarget == access::target::host_image && ( accessMode == // access::mode::read || accessMode == access::mode::read_write)) template 0) && (IsValidCoordDataT::value) && ((IsImageAcc && IsImageAccessReadOnly) || (IsHostImageAcc && IsImageAccessAnyRead))>> @@ -859,7 +856,7 @@ class image_accessor // access::mode::write || accessMode == access::mode::discard_write || // accessMode == access::mode::read_write)) template 0) && (detail::is_genint::value) && (IsValidCoordDataT::value) && ((IsImageAcc && IsImageAccessWriteOnly) || @@ -915,22 +912,22 @@ class __image_array_slice__ { : MBaseAcc(BaseAcc), MIdx(Idx) {} template 0) && (IsValidCoordDataT::value)>> DataT read(const CoordT &Coords) const { return MBaseAcc.read(getAdjustedCoords(Coords)); } template 0) && IsValidCoordDataT::value>> + typename = std::enable_if_t<(Dims > 0) && + IsValidCoordDataT::value>> DataT read(const CoordT &Coords, const sampler &Smpl) const { return MBaseAcc.read(getAdjustedCoords(Coords), Smpl); } template 0) && IsValidCoordDataT::value>> + typename = std::enable_if_t<(Dims > 0) && + IsValidCoordDataT::value>> void write(const CoordT &Coords, const DataT &Color) const { return MBaseAcc.write(getAdjustedCoords(Coords), Color); } @@ -940,12 +937,12 @@ class __image_array_slice__ { size_t get_count() const { return size(); } size_t size() const noexcept { return get_range().size(); } - template > + template > range<1> get_range() const { cl_int2 Count = MBaseAcc.getRangeInternal(); return range<1>(Count.x()); } - template > + template > range<2> get_range() const { cl_int3 Count = MBaseAcc.getRangeInternal(); return range<2>(Count.x(), Count.y()); @@ -960,7 +957,7 @@ class __image_array_slice__ { } template > + typename = std::enable_if_t<(Dims == 1 || Dims == 2)>> range get_range() const { return detail::convertToArrayOfN(MBaseAcc.getAccessRange()); } @@ -1269,7 +1266,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : public: template ::value && std::is_same::value && Dims == 0 && ((!IsPlaceH && IsHostBuf) || @@ -1301,7 +1298,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && std::is_same::value && Dims == 0 && ((!IsPlaceH && IsHostBuf) || @@ -1333,7 +1330,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : } template ::value && std::is_same::value && (Dims == 0) && (!IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf))>> @@ -1365,7 +1362,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && std::is_same::value && (Dims == 0) && (!IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf))>> @@ -1397,7 +1394,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : #endif template ::value && IsSameAsBuffer::value && ((!IsPlaceH && IsHostBuf) || @@ -1431,7 +1428,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && ((!IsPlaceH && IsHostBuf) || @@ -1468,7 +1465,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf)>> @@ -1482,7 +1479,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf)>> @@ -1497,7 +1494,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : #endif template ::value && IsSameAsBuffer::value && (!IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf))>> @@ -1530,7 +1527,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && (!IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf))>> @@ -1566,7 +1563,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && !IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf)>> @@ -1580,7 +1577,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && !IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf)>> @@ -1597,7 +1594,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : #endif template ::value && IsSameAsBuffer::value && ((!IsPlaceH && IsHostBuf) || @@ -1610,7 +1607,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && ((!IsPlaceH && IsHostBuf) || @@ -1626,7 +1623,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && IsPlaceH && (IsGlobalBuf || IsConstantBuf)>> @@ -1640,7 +1637,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && IsPlaceH && (IsGlobalBuf || IsConstantBuf)>> @@ -1656,7 +1653,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : #endif template ::value && IsSameAsBuffer::value && (!IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf))>> @@ -1669,7 +1666,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && (!IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf))>> @@ -1686,7 +1683,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && !IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf)>> @@ -1702,7 +1699,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && !IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf)>> @@ -1719,7 +1716,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : #endif template ::value && IsSameAsBuffer::value && ((!IsPlaceH && IsHostBuf) || @@ -1760,7 +1757,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && ((!IsPlaceH && IsHostBuf) || @@ -1805,7 +1802,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && IsPlaceH && (IsGlobalBuf || IsConstantBuf)>> @@ -1819,7 +1816,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && IsPlaceH && (IsGlobalBuf || IsConstantBuf)>> @@ -1835,7 +1832,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : #endif template ::value && IsSameAsBuffer::value && (!IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf))>> @@ -1876,7 +1873,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && (!IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf))>> @@ -1920,7 +1917,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && !IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf)>> @@ -1936,7 +1933,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : template ::value && IsSameAsBuffer::value && IsValidTag::value && !IsPlaceH && (IsGlobalBuf || IsConstantBuf || IsHostBuf)>> @@ -1997,12 +1994,12 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : bool empty() const noexcept { return size() == 0; } - template 0)>> + template 0)>> range get_range() const { return detail::convertToArrayOfN(getAccessRange()); } - template 0)>> + template 0)>> id get_offset() const { #if __cplusplus >= 201703L static_assert( @@ -2014,51 +2011,51 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : } template ::value>> + typename = std::enable_if_t::value>> operator RefType() const { const size_t LinearIndex = getLinearIndex(id()); return *(getQualifiedPtr() + LinearIndex); } template > + typename = std::enable_if_t> operator ConstRefType() const { const size_t LinearIndex = getLinearIndex(id()); return *(getQualifiedPtr() + LinearIndex); } template 0) && IsAccessAnyWrite>> + typename = std::enable_if_t<(Dims > 0) && IsAccessAnyWrite>> RefType operator[](id Index) const { const size_t LinearIndex = getLinearIndex(Index); return getQualifiedPtr()[LinearIndex]; } template - typename detail::enable_if_t<(Dims > 0) && IsAccessReadOnly, ConstRefType> + typename std::enable_if_t<(Dims > 0) && IsAccessReadOnly, ConstRefType> operator[](id Index) const { const size_t LinearIndex = getLinearIndex(Index); return getQualifiedPtr()[LinearIndex]; } template - operator typename detail::enable_if_t + atomic #else - atomic + atomic #endif - >() const { + >() const { const size_t LinearIndex = getLinearIndex(id()); return atomic(multi_ptr( getQualifiedPtr() + LinearIndex)); } template - typename detail::enable_if_t<(Dims > 0) && AccessMode == access::mode::atomic, - atomic> + typename std::enable_if_t<(Dims > 0) && AccessMode == access::mode::atomic, + atomic> operator[](id Index) const { const size_t LinearIndex = getLinearIndex(Index); return atomic(multi_ptr( @@ -2066,35 +2063,35 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : } template - typename detail::enable_if_t> + typename std::enable_if_t> operator[](size_t Index) const { const size_t LinearIndex = getLinearIndex(id(Index)); return atomic(multi_ptr( getQualifiedPtr() + LinearIndex)); } - template 1)>> + template 1)>> auto operator[](size_t Index) const { return AccessorSubscript(*this, Index); } - template > + template < + access::target AccessTarget_ = AccessTarget, + typename = std::enable_if_t> DataT *get_pointer() const { return getPointerAdjusted(); } template < access::target AccessTarget_ = AccessTarget, - typename = detail::enable_if_t> + typename = std::enable_if_t> global_ptr get_pointer() const { return global_ptr(getPointerAdjusted()); } template > + typename = std::enable_if_t> constant_ptr get_pointer() const { return constant_ptr(getPointerAdjusted()); } @@ -2103,7 +2100,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : // code. This restriction is not listed in the core spec and will be added in // future versions. template - typename sycl::detail::enable_if_t< + typename std::enable_if_t< !ext::oneapi::is_compile_time_property::value, bool> has_property() const noexcept { #ifndef __SYCL_DEVICE_ONLY__ @@ -2117,7 +2114,7 @@ class __SYCL_SPECIAL_CLASS __SYCL_TYPE(accessor) accessor : // code. This restriction is not listed in the core spec and will be added in // future versions. template ::value>> Property get_property() const { #ifndef __SYCL_DEVICE_ONLY__ @@ -2506,7 +2503,7 @@ class __SYCL_SPECIAL_CLASS local_accessor_base : using reference = DataT &; using const_reference = const DataT &; - template > + template > local_accessor_base(handler &, const detail::code_location CodeLoc = detail::code_location::current()) #ifdef __SYCL_DEVICE_ONLY__ @@ -2519,8 +2516,7 @@ class __SYCL_SPECIAL_CLASS local_accessor_base : } #endif - template > + template > local_accessor_base(handler &, const property_list &propList, const detail::code_location CodeLoc = detail::code_location::current()) @@ -2537,7 +2533,7 @@ class __SYCL_SPECIAL_CLASS local_accessor_base : } #endif - template 0)>> + template 0)>> local_accessor_base( range AllocationSize, handler &, const detail::code_location CodeLoc = detail::code_location::current()) @@ -2553,7 +2549,7 @@ class __SYCL_SPECIAL_CLASS local_accessor_base : #endif template 0)>> + typename = std::enable_if_t<(Dims > 0)>> local_accessor_base(range AllocationSize, handler &, const property_list &propList, const detail::code_location CodeLoc = @@ -2577,32 +2573,32 @@ class __SYCL_SPECIAL_CLASS local_accessor_base : size_t get_count() const { return size(); } size_t size() const noexcept { return getSize().size(); } - template 0)>> + template 0)>> range get_range() const { return detail::convertToArrayOfN(getSize()); } template > + typename = std::enable_if_t> operator RefType() const { return *getQualifiedPtr(); } template 0) && IsAccessAnyWrite>> + typename = std::enable_if_t<(Dims > 0) && IsAccessAnyWrite>> RefType operator[](id Index) const { const size_t LinearIndex = getLinearIndex(Index); return getQualifiedPtr()[LinearIndex]; } template > + typename = std::enable_if_t> RefType operator[](size_t Index) const { return getQualifiedPtr()[Index]; } template - operator typename detail::enable_if_t< + operator typename std::enable_if_t< Dims == 0 && AccessMode == access::mode::atomic, atomic>() const { return atomic( @@ -2610,8 +2606,8 @@ class __SYCL_SPECIAL_CLASS local_accessor_base : } template - typename detail::enable_if_t<(Dims > 0) && AccessMode == access::mode::atomic, - atomic> + typename std::enable_if_t<(Dims > 0) && AccessMode == access::mode::atomic, + atomic> operator[](id Index) const { const size_t LinearIndex = getLinearIndex(Index); return atomic(multi_ptr( @@ -2619,14 +2615,14 @@ class __SYCL_SPECIAL_CLASS local_accessor_base : } template - typename detail::enable_if_t> + typename std::enable_if_t> operator[](size_t Index) const { return atomic(multi_ptr( getQualifiedPtr() + Index)); } - template 1)>> + template 1)>> typename AccessorCommonT::template AccessorSubscript< Dims - 1, local_accessor_base> @@ -2993,7 +2989,7 @@ class host_accessor // -------+---------+-------+----+----------+-------------- template ::value && Dims == 0>> host_accessor( buffer &BufferRef, @@ -3002,7 +2998,7 @@ class host_accessor : AccessorT(BufferRef, PropertyList, CodeLoc) {} template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, const property_list &PropertyList = {}, @@ -3012,7 +3008,7 @@ class host_accessor #if __cplusplus >= 201703L template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, mode_tag_t, const property_list &PropertyList = {}, @@ -3022,7 +3018,7 @@ class host_accessor #endif template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, handler &CommandGroupHandler, const property_list &PropertyList = {}, @@ -3032,7 +3028,7 @@ class host_accessor #if __cplusplus >= 201703L template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, handler &CommandGroupHandler, mode_tag_t, @@ -3043,7 +3039,7 @@ class host_accessor #endif template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, range AccessRange, const property_list &PropertyList = {}, @@ -3053,7 +3049,7 @@ class host_accessor #if __cplusplus >= 201703L template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, range AccessRange, mode_tag_t, @@ -3064,7 +3060,7 @@ class host_accessor #endif template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, handler &CommandGroupHandler, range AccessRange, @@ -3076,7 +3072,7 @@ class host_accessor #if __cplusplus >= 201703L template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, handler &CommandGroupHandler, range AccessRange, @@ -3088,7 +3084,7 @@ class host_accessor #endif template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, range AccessRange, id AccessOffset, @@ -3100,7 +3096,7 @@ class host_accessor #if __cplusplus >= 201703L template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, range AccessRange, id AccessOffset, @@ -3112,7 +3108,7 @@ class host_accessor #endif template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, handler &CommandGroupHandler, range AccessRange, @@ -3124,7 +3120,7 @@ class host_accessor #if __cplusplus >= 201703L template ::value>> + typename = std::enable_if_t::value>> host_accessor( buffer &BufferRef, handler &CommandGroupHandler, range AccessRange, diff --git a/sycl/include/sycl/atomic.hpp b/sycl/include/sycl/atomic.hpp index 697907dc0c45b..beb9174941e30 100644 --- a/sycl/include/sycl/atomic.hpp +++ b/sycl/include/sycl/atomic.hpp @@ -210,7 +210,7 @@ class __SYCL2020_DEPRECATED( #ifdef __ENABLE_USM_ADDR_SPACE__ // Create atomic in global_space with one from ext_intel_global_device_space template > atomic(const atomic @@ -219,7 +219,7 @@ class __SYCL2020_DEPRECATED( } template > atomic( @@ -235,13 +235,13 @@ class __SYCL2020_DEPRECATED( #ifdef __SYCL_DEVICE_ONLY__ template - detail::enable_if_t::value, T> + std::enable_if_t::value, T> load(memory_order Order = memory_order::relaxed) const { return __spirv_AtomicLoad(Ptr, SpirvScope, detail::getSPIRVMemorySemanticsMask(Order)); } template - detail::enable_if_t::value, T> + std::enable_if_t::value, T> load(memory_order Order = memory_order::relaxed) const { auto *TmpPtr = reinterpret_cast::pointer>(Ptr); diff --git a/sycl/include/sycl/atomic_ref.hpp b/sycl/include/sycl/atomic_ref.hpp index cbae52de9d7c7..f20549f847e58 100644 --- a/sycl/include/sycl/atomic_ref.hpp +++ b/sycl/include/sycl/atomic_ref.hpp @@ -89,7 +89,7 @@ inline constexpr memory_order getLoadOrder(memory_order order) { template struct bit_equal; template -struct bit_equal::value>> { +struct bit_equal::value>> { bool operator()(const T &lhs, const T &rhs) { return lhs == rhs; } }; @@ -266,7 +266,7 @@ class atomic_ref_impl template class atomic_ref_impl::value>> + typename std::enable_if_t::value>> : public atomic_ref_base { public: @@ -414,7 +414,7 @@ template class atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, - typename detail::enable_if_t::value>> + typename std::enable_if_t::value>> : public atomic_ref_base { public: diff --git a/sycl/include/sycl/backend/opencl.hpp b/sycl/include/sycl/backend/opencl.hpp index f60dddd4b1d8d..bbf06d3a1eddc 100644 --- a/sycl/include/sycl/backend/opencl.hpp +++ b/sycl/include/sycl/backend/opencl.hpp @@ -33,7 +33,7 @@ __SYCL_EXPORT bool has_extension(const sycl::device &SyclDevice, const std::string &Extension); // Construction of SYCL platform. -template ::value> * = nullptr> __SYCL_DEPRECATED("Use SYCL 2020 sycl::make_platform free function") T make(typename detail::interop::type Interop) { @@ -41,24 +41,24 @@ T make(typename detail::interop::type Interop) { } // Construction of SYCL device. -template ::value> * = nullptr> +template ::value> * = nullptr> __SYCL_DEPRECATED("Use SYCL 2020 sycl::make_device free function") T make(typename detail::interop::type Interop) { return make_device(detail::pi::cast(Interop)); } // Construction of SYCL context. -template ::value> * = nullptr> +template ::value> + * = nullptr> __SYCL_DEPRECATED("Use SYCL 2020 sycl::make_context free function") T make(typename detail::interop::type Interop) { return make_context(detail::pi::cast(Interop)); } // Construction of SYCL queue. -template ::value> * = nullptr> +template ::value> * = nullptr> __SYCL_DEPRECATED("Use SYCL 2020 sycl::make_queue free function") T make(const context &Context, typename detail::interop::type Interop) { diff --git a/sycl/include/sycl/buffer.hpp b/sycl/include/sycl/buffer.hpp index 6152cd596fa60..5e115c4f3643a 100644 --- a/sycl/include/sycl/buffer.hpp +++ b/sycl/include/sycl/buffer.hpp @@ -140,8 +140,8 @@ class __SYCL_EXPORT buffer_plain { /// \ingroup sycl_api template >, - typename __Enabled = typename detail::enable_if_t<(dimensions > 0) && - (dimensions <= 3)>> + typename __Enabled = + typename std::enable_if_t<(dimensions > 0) && (dimensions <= 3)>> class buffer : public detail::buffer_plain, public detail::OwnerLessBase> { // TODO check is_device_copyable::value after converting sycl::vec into a @@ -155,21 +155,21 @@ class buffer : public detail::buffer_plain, using const_reference = const value_type &; using allocator_type = AllocatorT; template - using EnableIfOneDimension = typename detail::enable_if_t<1 == dims>; + using EnableIfOneDimension = typename std::enable_if_t<1 == dims>; // using same requirement for contiguous container as std::span template using EnableIfContiguous = - detail::void_t().data())> (*)[], const T (*)[]>::value>, decltype(std::declval().size())>; template - using EnableIfItInputIterator = detail::enable_if_t< + using EnableIfItInputIterator = std::enable_if_t< std::is_convertible::iterator_category, std::input_iterator_tag>::value>; template - using EnableIfSameNonConstIterators = typename detail::enable_if_t< + using EnableIfSameNonConstIterators = typename std::enable_if_t< std::is_same::value && !std::is_const::value, ItA>; std::array rangeToArray(range<3> &r) { return {r[0], r[1], r[2]}; } @@ -579,7 +579,7 @@ class buffer : public detail::buffer_plain, } template