From 73c6b125f6a558f799473fc25f3af6b4241ed049 Mon Sep 17 00:00:00 2001 From: Andrei Elovikov Date: Wed, 27 Mar 2024 12:32:25 -0700 Subject: [PATCH] [ABI-Break][SYCL] Enable "Neutral" ABI in regards to C++11 ABI by default --- sycl/include/sycl/detail/util.hpp | 11 +- sycl/include/sycl/device.hpp | 11 - sycl/include/sycl/exception.hpp | 13 - sycl/include/sycl/handler.hpp | 21 -- sycl/include/sycl/kernel.hpp | 8 - sycl/include/sycl/kernel_bundle.hpp | 9 - sycl/include/sycl/platform.hpp | 20 +- sycl/source/device.cpp | 28 -- sycl/source/exception.cpp | 20 -- sycl/source/handler.cpp | 36 -- sycl/source/kernel.cpp | 10 - sycl/source/kernel_bundle.cpp | 4 - sycl/source/platform.cpp | 10 - sycl/test/abi/sycl_symbols_linux.dump | 314 +++++++++--------- sycl/test/abi/symbol_size_alignment.cpp | 2 +- .../arg_mask/EliminatedArgMask.cpp | 4 - .../scheduler/SchedulerTestUtils.hpp | 4 - 17 files changed, 159 insertions(+), 366 deletions(-) diff --git a/sycl/include/sycl/detail/util.hpp b/sycl/include/sycl/detail/util.hpp index 4b831e2e38e8f..67f37f0ffc4ec 100644 --- a/sycl/include/sycl/detail/util.hpp +++ b/sycl/include/sycl/detail/util.hpp @@ -10,12 +10,10 @@ #ifndef __SYCL_DEVICE_ONLY -#include -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES -#include -#endif #include #include +#include +#include #include namespace sycl { @@ -69,7 +67,6 @@ struct CmpCStr { using SerializedObj = std::vector; -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES template struct ABINeutralT { using type = T; }; // We need special handling of std::string to handle ABI incompatibility // for get_info<>() when it returns std::string and vector. @@ -85,10 +82,6 @@ template <> struct ABINeutralT> { }; template using ABINeutralT_t = typename ABINeutralT::type; -#else -template using ABINeutralT_t = T; -#endif - } // namespace detail } // namespace _V1 } // namespace sycl diff --git a/sycl/include/sycl/device.hpp b/sycl/include/sycl/device.hpp index 3f8dc33b5dd4f..35b253ed7d2e4 100644 --- a/sycl/include/sycl/device.hpp +++ b/sycl/include/sycl/device.hpp @@ -15,10 +15,8 @@ #include #include #include -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES #include #include -#endif #include #include #include @@ -221,17 +219,10 @@ class __SYCL_EXPORT device : public detail::OwnerLessBase { /// type associated with the param parameter. /// /// \return device info of type described in Table 4.20. -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES template typename detail::is_device_info_desc::return_type get_info() const { return detail::convert_from_abi_neutral(get_info_impl()); } -#else - template - detail::ABINeutralT_t< - typename detail::is_device_info_desc::return_type> - get_info() const; -#endif /// Check SYCL extension support by device /// @@ -370,12 +361,10 @@ class __SYCL_EXPORT device : public detail::OwnerLessBase { friend auto get_native(const SyclObjectT &Obj) -> backend_return_t; -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES template typename detail::ABINeutralT_t< typename detail::is_device_info_desc::return_type> get_info_impl() const; -#endif }; } // namespace _V1 diff --git a/sycl/include/sycl/exception.hpp b/sycl/include/sycl/exception.hpp index 59bbd9bcdf774..ea108f43b3463 100644 --- a/sycl/include/sycl/exception.hpp +++ b/sycl/include/sycl/exception.hpp @@ -74,21 +74,13 @@ class __SYCL_EXPORT exception : public virtual std::exception { exception(std::error_code, const char *Msg); -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES exception(std::error_code Ec, const std::string &Msg) : exception(Ec, nullptr, Msg.c_str()) {} -#else - exception(std::error_code, const std::string &Msg); -#endif // new SYCL 2020 constructors exception(std::error_code); -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES exception(int EV, const std::error_category &ECat, const std::string &WhatArg) : exception(EV, ECat, WhatArg.c_str()) {} -#else - exception(int, const std::error_category &, const std::string &); -#endif exception(int, const std::error_category &, const char *); exception(int, const std::error_category &); @@ -137,16 +129,11 @@ class __SYCL_EXPORT exception : public virtual std::exception { // base constructor for all SYCL 2020 constructors // exception(context *ctxPtr, std::error_code Ec, const std::string // &what_arg); -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES exception(std::error_code Ec, std::shared_ptr SharedPtrCtx, const std::string &what_arg) : exception(Ec, SharedPtrCtx, what_arg.c_str()) {} exception(std::error_code Ec, std::shared_ptr SharedPtrCtx, const char *WhatArg); -#else - exception(std::error_code Ec, std::shared_ptr SharedPtrCtx, - const std::string &what_arg); -#endif }; class __SYCL2020_DEPRECATED( diff --git a/sycl/include/sycl/handler.hpp b/sycl/include/sycl/handler.hpp index 772f09773b561..614ad7738e098 100644 --- a/sycl/include/sycl/handler.hpp +++ b/sycl/include/sycl/handler.hpp @@ -21,10 +21,8 @@ #include #include #include -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES #include #include -#endif #include #include #include @@ -422,11 +420,6 @@ template bool range_size_fits_in_size_t(const range &r) { } return true; } -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES -using string = std::string; -using string_view = std::string; -#endif - } // namespace detail /// Command group handler class. @@ -872,14 +865,10 @@ class __SYCL_EXPORT handler { /// /// \param KernelName is the name of the SYCL kernel to check that the used /// kernel bundle contains. -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES void verifyUsedKernelBundle(const std::string &KernelName) { verifyUsedKernelBundleInternal(detail::string_view{KernelName}); } void verifyUsedKernelBundleInternal(detail::string_view KernelName); -#else - void verifyUsedKernelBundle(const std::string &KernelName); -#endif /// Stores lambda to the template-free object /// @@ -3390,17 +3379,12 @@ class __SYCL_EXPORT handler { /// expr m_Storage member /// \param Size the size of data getting read back / to. /// \param Block if read operation is blocking, default to false. -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES void ext_intel_read_host_pipe(const std::string &Name, void *Ptr, size_t Size, bool Block = false) { ext_intel_read_host_pipe(detail::string_view(Name), Ptr, Size, Block); } void ext_intel_read_host_pipe(detail::string_view Name, void *Ptr, size_t Size, bool Block = false); -#else - void ext_intel_read_host_pipe(const std::string &Name, void *Ptr, size_t Size, - bool Block = false); -#endif /// Write to host pipes given a host address and /// \param Name name of the host pipe to be passed into lower level runtime @@ -3408,17 +3392,12 @@ class __SYCL_EXPORT handler { /// expr m_Storage member /// \param Size the size of data getting read back / to. /// \param Block if write opeartion is blocking, default to false. -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES void ext_intel_write_host_pipe(const std::string &Name, void *Ptr, size_t Size, bool Block = false) { ext_intel_write_host_pipe(detail::string_view(Name), Ptr, Size, Block); } void ext_intel_write_host_pipe(detail::string_view Name, void *Ptr, size_t Size, bool Block = false); -#else - void ext_intel_write_host_pipe(const std::string &Name, void *Ptr, - size_t Size, bool Block = false); -#endif friend class ext::oneapi::experimental::detail::graph_impl; friend class ext::oneapi::experimental::detail::dynamic_parameter_impl; diff --git a/sycl/include/sycl/kernel.hpp b/sycl/include/sycl/kernel.hpp index 6cc7c3c3da215..38ee8d18b079b 100644 --- a/sycl/include/sycl/kernel.hpp +++ b/sycl/include/sycl/kernel.hpp @@ -15,10 +15,8 @@ #include // for is_kernel_device_specif... #include // for OwnerLessBase #include // for pi_native_handle -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES #include #include -#endif #include #include // for device #include // for bundle_state @@ -142,13 +140,9 @@ class __SYCL_EXPORT kernel : public detail::OwnerLessBase { /// /// \return depends on information being queried. template -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES typename detail::is_kernel_info_desc::return_type get_info() const { return detail::convert_from_abi_neutral(get_info_impl()); } -#else - typename detail::is_kernel_info_desc::return_type get_info() const; -#endif /// Query device-specific information from the kernel object using the /// info::kernel_device_specific descriptor. @@ -194,12 +188,10 @@ class __SYCL_EXPORT kernel : public detail::OwnerLessBase { template friend auto get_native(const SyclObjectT &Obj) -> backend_return_t; -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES template typename detail::ABINeutralT_t< typename detail::is_kernel_info_desc::return_type> get_info_impl() const; -#endif }; } // namespace _V1 } // namespace sycl diff --git a/sycl/include/sycl/kernel_bundle.hpp b/sycl/include/sycl/kernel_bundle.hpp index 6114defc47f21..efd22f6dbb337 100644 --- a/sycl/include/sycl/kernel_bundle.hpp +++ b/sycl/include/sycl/kernel_bundle.hpp @@ -15,9 +15,7 @@ #include // for OwnerLessBase #include // for pi_native_handle #include // for cast -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES #include -#endif #include // for device #include // for kernel, kernel_bundle #include // for bundle_state @@ -450,9 +448,6 @@ kernel_bundle(kernel_bundle &&) -> kernel_bundle; ///////////////////////// namespace detail { -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES -using string_view = std::string; -#endif // Internal non-template versions of get_kernel_id API which is used by public // onces __SYCL_EXPORT kernel_id get_kernel_id_impl(string_view KernelName); @@ -463,11 +458,7 @@ template kernel_id get_kernel_id() { // FIXME: This must fail at link-time if KernelName not in any available // translation units. using KI = sycl::detail::KernelInfo; -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES return detail::get_kernel_id_impl(detail::string_view{KI::getName()}); -#else - return detail::get_kernel_id_impl(KI::getName()); -#endif } /// \returns a vector with all kernel_id's defined in the application diff --git a/sycl/include/sycl/platform.hpp b/sycl/include/sycl/platform.hpp index 32a93acd0a873..546fdf0683957 100644 --- a/sycl/include/sycl/platform.hpp +++ b/sycl/include/sycl/platform.hpp @@ -16,10 +16,8 @@ #include #include #include -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES #include #include -#endif #include #include #include @@ -58,7 +56,6 @@ class platform_impl; void __SYCL_EXPORT enable_ext_oneapi_default_context(bool Val); template auto convert_to_abi_neutral(ParamT &&Info) { -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES using ParamNoRef = std::remove_reference_t; if constexpr (std::is_same_v) { return detail::string{Info}; @@ -72,13 +69,9 @@ template auto convert_to_abi_neutral(ParamT &&Info) { } else { return std::forward(Info); } -#else - return std::forward(Info); -#endif } template auto convert_from_abi_neutral(ParamT &&Info) { -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES using ParamNoRef = std::remove_reference_t; if constexpr (std::is_same_v) { return Info.c_str(); @@ -93,9 +86,6 @@ template auto convert_from_abi_neutral(ParamT &&Info) { } else { return std::forward(Info); } -#else - return std::forward(Info); -#endif } } // namespace detail namespace ext::oneapi { @@ -190,17 +180,11 @@ class __SYCL_EXPORT platform : public detail::OwnerLessBase { /// Queries this SYCL platform for info. /// /// The return type depends on information being queried. -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES template typename detail::is_platform_info_desc::return_type get_info() const { return detail::convert_from_abi_neutral(get_info_impl()); } -#else - template - detail::ABINeutralT_t< - typename detail::is_platform_info_desc::return_type> - get_info() const; -#endif + /// Returns all available SYCL platforms in the system. /// /// The resulting vector always contains a single SYCL host platform instance. @@ -261,12 +245,10 @@ class __SYCL_EXPORT platform : public detail::OwnerLessBase { friend auto get_native(const SyclObjectT &Obj) -> backend_return_t; -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES template typename detail::ABINeutralT_t< typename detail::is_platform_info_desc::return_type> get_info_impl() const; -#endif }; // class platform } // namespace _V1 } // namespace sycl diff --git a/sycl/source/device.cpp b/sycl/source/device.cpp index 4d9737ca0412a..17b74baf841e0 100644 --- a/sycl/source/device.cpp +++ b/sycl/source/device.cpp @@ -135,22 +135,14 @@ bool device::has_extension(const std::string &extension_name) const { template detail::ABINeutralT_t::return_type> -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES device::get_info_impl() const { -#else -device::get_info() const { -#endif return detail::convert_to_abi_neutral(impl->template get_info()); } // Explicit override. Not fulfilled by #include device_traits.def below. template <> -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES __SYCL_EXPORT device device::get_info_impl() const { -#else -__SYCL_EXPORT device device::get_info() const { -#endif // With ONEAPI_DEVICE_SELECTOR the impl.MRootDevice is preset and may be // overridden (ie it may be nullptr on a sub-device) The PI of the sub-devices // have parents, but we don't want to return them. They must pretend to be @@ -165,11 +157,7 @@ __SYCL_EXPORT device device::get_info() const { template <> __SYCL_EXPORT std::vector -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES device::get_info_impl() const { -#else -device::get_info() const { -#endif std::vector DeviceAspects{ #define __SYCL_ASPECT(ASPECT, ID) aspect::ASPECT, #include @@ -193,25 +181,15 @@ device::get_info() const { } template <> -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES __SYCL_EXPORT bool device::get_info_impl() const { -#else -__SYCL_EXPORT bool device::get_info() const { -#endif // Explicit specialization is needed due to the class of info handle. The // implementation is done in get_device_info_impl. return impl->template get_info(); } -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES #define __SYCL_PARAM_TRAITS_SPEC(DescType, Desc, ReturnT, PiCode) \ template __SYCL_EXPORT detail::ABINeutralT_t \ device::get_info_impl() const; -#else -#define __SYCL_PARAM_TRAITS_SPEC(DescType, Desc, ReturnT, PiCode) \ - template __SYCL_EXPORT detail::ABINeutralT_t \ - device::get_info() const; -#endif #define __SYCL_PARAM_TRAITS_SPEC_SPECIALIZED(DescType, Desc, ReturnT, PiCode) @@ -219,15 +197,9 @@ __SYCL_EXPORT bool device::get_info() const { #undef __SYCL_PARAM_TRAITS_SPEC_SPECIALIZED #undef __SYCL_PARAM_TRAITS_SPEC -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES #define __SYCL_PARAM_TRAITS_SPEC(Namespace, DescType, Desc, ReturnT, PiCode) \ template __SYCL_EXPORT detail::ABINeutralT_t \ device::get_info_impl() const; -#else -#define __SYCL_PARAM_TRAITS_SPEC(Namespace, DescType, Desc, ReturnT, PiCode) \ - template __SYCL_EXPORT typename detail::ABINeutralT_t \ - device::get_info() const; -#endif #include #include diff --git a/sycl/source/exception.cpp b/sycl/source/exception.cpp index ad1d39e3dae18..595f25c5d8aa2 100644 --- a/sycl/source/exception.cpp +++ b/sycl/source/exception.cpp @@ -19,20 +19,9 @@ inline namespace _V1 { exception::exception(std::error_code EC, const char *Msg) : exception(EC, nullptr, Msg) {} -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES -exception::exception(std::error_code EC, const std::string &Msg) - : exception(EC, nullptr, Msg) {} -#endif - // new SYCL 2020 constructors exception::exception(std::error_code EC) : exception(EC, nullptr, "") {} -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES -exception::exception(int EV, const std::error_category &ECat, - const std::string &WhatArg) - : exception({EV, ECat}, nullptr, WhatArg) {} -#endif - exception::exception(int EV, const std::error_category &ECat, const char *WhatArg) : exception({EV, ECat}, nullptr, std::string(WhatArg)) {} @@ -62,21 +51,12 @@ exception::exception(context Ctx, int EV, const std::error_category &ECat) : exception(Ctx, EV, ECat, "") {} // protected base constructor for all SYCL 2020 constructors -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES exception::exception(std::error_code EC, std::shared_ptr SharedPtrCtx, const char *WhatArg) : MMsg(std::make_shared(WhatArg)), MPIErr(PI_ERROR_INVALID_VALUE), MContext(SharedPtrCtx), MErrC(EC) { detail::GlobalHandler::instance().TraceEventXPTI(MMsg->c_str()); } -#else -exception::exception(std::error_code EC, std::shared_ptr SharedPtrCtx, - const std::string &WhatArg) - : MMsg(std::make_shared(WhatArg)), - MPIErr(PI_ERROR_INVALID_VALUE), MContext(SharedPtrCtx), MErrC(EC) { - detail::GlobalHandler::instance().TraceEventXPTI(MMsg->c_str()); -} -#endif exception::~exception() {} diff --git a/sycl/source/handler.cpp b/sycl/source/handler.cpp index e5c2f97d3ccb6..17cde0994b314 100644 --- a/sycl/source/handler.cpp +++ b/sycl/source/handler.cpp @@ -197,12 +197,8 @@ event handler::finalize() { !MImpl->isStateExplicitKernelBundle()) { auto Dev = MGraph ? MGraph->getDevice() : MQueue->get_device(); kernel_id KernelID = -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES detail::ProgramManager::getInstance().getSYCLKernelID( MKernelName.c_str()); -#else - detail::ProgramManager::getInstance().getSYCLKernelID(MKernelName); -#endif bool KernelInserted = KernelBundleImpPtr->add_kernel(KernelID, Dev); // If kernel was not inserted and the bundle is in input mode we try // building it and trying to find the kernel in executable mode @@ -261,11 +257,7 @@ event handler::finalize() { // uint32_t StreamID, uint64_t InstanceID, xpti_td* TraceEvent, int32_t StreamID = xptiRegisterStream(detail::SYCL_STREAM_NAME); auto [CmdTraceEvent, InstanceID] = emitKernelInstrumentationData( -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES StreamID, MKernel, MCodeLoc, MKernelName.c_str(), MQueue, MNDRDesc, -#else - StreamID, MKernel, MCodeLoc, MKernelName, MQueue, MNDRDesc, -#endif KernelBundleImpPtr, MArgs); auto EnqueueKernel = [&, CmdTraceEvent = CmdTraceEvent, InstanceID = InstanceID]() { @@ -315,11 +307,7 @@ event handler::finalize() { } else { Result = enqueueImpKernel( MQueue, MNDRDesc, MArgs, KernelBundleImpPtr, MKernel, -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES MKernelName.c_str(), RawEvents, NewEvent, nullptr, -#else - MKernelName, RawEvents, NewEvent, nullptr, -#endif MImpl->MKernelCacheConfig, MImpl->MKernelIsCooperative); } } @@ -341,12 +329,8 @@ event handler::finalize() { // Kernel only uses assert if it's non interop one bool KernelUsesAssert = !(MKernel && MKernel->isInterop()) && -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES detail::ProgramManager::getInstance().kernelUsesAssert( MKernelName.c_str()); -#else - detail::ProgramManager::getInstance().kernelUsesAssert(MKernelName); -#endif DiscardEvent = !KernelUsesAssert; } @@ -382,11 +366,7 @@ event handler::finalize() { CommandGroup.reset(new detail::CGExecKernel( std::move(MNDRDesc), std::move(MHostKernel), std::move(MKernel), std::move(MImpl->MKernelBundle), std::move(CGData), std::move(MArgs), -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES MKernelName.c_str(), std::move(MStreamStorage), -#else - MKernelName, std::move(MStreamStorage), -#endif std::move(MImpl->MAuxiliaryResources), MCGType, MImpl->MKernelCacheConfig, MImpl->MKernelIsCooperative, MCodeLoc)); break; @@ -918,11 +898,7 @@ detail::string handler::getKernelName() { return detail::string{MKernel->get_info()}; } -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES void handler::verifyUsedKernelBundleInternal(detail::string_view KernelName) { -#else -void handler::verifyUsedKernelBundle(const std::string &KernelName) { -#endif auto UsedKernelBundleImplPtr = getOrInsertHandlerKernelBundle(/*Insert=*/false); if (!UsedKernelBundleImplPtr) @@ -1437,15 +1413,9 @@ id<2> handler::computeFallbackKernelBounds(size_t Width, size_t Height) { return id<2>{std::min(ItemLimit[0], Height), std::min(ItemLimit[1], Width)}; } -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES void handler::ext_intel_read_host_pipe(detail::string_view Name, void *Ptr, size_t Size, bool Block) { MImpl->HostPipeName = Name.data(); -#else -void handler::ext_intel_read_host_pipe(const std::string &Name, void *Ptr, - size_t Size, bool Block) { - MImpl->HostPipeName = Name; -#endif MImpl->HostPipePtr = Ptr; MImpl->HostPipeTypeSize = Size; MImpl->HostPipeBlocking = Block; @@ -1453,15 +1423,9 @@ void handler::ext_intel_read_host_pipe(const std::string &Name, void *Ptr, setType(detail::CG::ReadWriteHostPipe); } -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES void handler::ext_intel_write_host_pipe(detail::string_view Name, void *Ptr, size_t Size, bool Block) { MImpl->HostPipeName = Name.data(); -#else -void handler::ext_intel_write_host_pipe(const std::string &Name, void *Ptr, - size_t Size, bool Block) { - MImpl->HostPipeName = Name; -#endif MImpl->HostPipePtr = Ptr; MImpl->HostPipeTypeSize = Size; MImpl->HostPipeBlocking = Block; diff --git a/sycl/source/kernel.cpp b/sycl/source/kernel.cpp index d981833f94958..92b005e2e4062 100644 --- a/sycl/source/kernel.cpp +++ b/sycl/source/kernel.cpp @@ -50,23 +50,13 @@ kernel::get_kernel_bundle() const { template detail::ABINeutralT_t::return_type> -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES kernel::get_info_impl() const { -#else -kernel::get_info() const { -#endif return detail::convert_to_abi_neutral(impl->template get_info()); } -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES #define __SYCL_PARAM_TRAITS_SPEC(DescType, Desc, ReturnT, PiCode) \ template __SYCL_EXPORT detail::ABINeutralT_t \ kernel::get_info_impl() const; -#else -#define __SYCL_PARAM_TRAITS_SPEC(DescType, Desc, ReturnT, PiCode) \ - template __SYCL_EXPORT detail::ABINeutralT_t \ - kernel::get_info() const; -#endif #include diff --git a/sycl/source/kernel_bundle.cpp b/sycl/source/kernel_bundle.cpp index 5fcad0af99ca3..32ec35dbee837 100644 --- a/sycl/source/kernel_bundle.cpp +++ b/sycl/source/kernel_bundle.cpp @@ -140,12 +140,8 @@ removeDuplicateDevices(const std::vector &Devs) { } kernel_id get_kernel_id_impl(string_view KernelName) { -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES return detail::ProgramManager::getInstance().getSYCLKernelID( KernelName.data()); -#else - return detail::ProgramManager::getInstance().getSYCLKernelID(KernelName); -#endif } detail::KernelBundleImplPtr diff --git a/sycl/source/platform.cpp b/sycl/source/platform.cpp index c991f27eda51b..eff1708431d1b 100644 --- a/sycl/source/platform.cpp +++ b/sycl/source/platform.cpp @@ -59,11 +59,7 @@ backend platform::get_backend() const noexcept { return impl->getBackend(); } template detail::ABINeutralT_t< typename detail::is_platform_info_desc::return_type> -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES platform::get_info_impl() const { -#else -platform::get_info() const { -#endif return detail::convert_to_abi_neutral(impl->template get_info()); } @@ -71,15 +67,9 @@ pi_native_handle platform::getNative() const { return impl->getNative(); } bool platform::has(aspect Aspect) const { return impl->has(Aspect); } -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES #define __SYCL_PARAM_TRAITS_SPEC(DescType, Desc, ReturnT, PiCode) \ template __SYCL_EXPORT detail::ABINeutralT_t \ platform::get_info_impl() const; -#else -#define __SYCL_PARAM_TRAITS_SPEC(DescType, Desc, ReturnT, PiCode) \ - template __SYCL_EXPORT detail::ABINeutralT_t \ - platform::get_info() const; -#endif #include #undef __SYCL_PARAM_TRAITS_SPEC diff --git a/sycl/test/abi/sycl_symbols_linux.dump b/sycl/test/abi/sycl_symbols_linux.dump index 8a5cbaa9bbac2..28db3de391d1b 100644 --- a/sycl/test/abi/sycl_symbols_linux.dump +++ b/sycl/test/abi/sycl_symbols_linux.dump @@ -4004,7 +4004,7 @@ _ZN4sycl3_V16detail17device_global_map3addEPKvPKc _ZN4sycl3_V16detail17reduComputeWGSizeEmmRm _ZN4sycl3_V16detail18convertChannelTypeE22_pi_image_channel_type _ZN4sycl3_V16detail18convertChannelTypeENS0_18image_channel_typeE -_ZN4sycl3_V16detail18get_kernel_id_implENSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE +_ZN4sycl3_V16detail18get_kernel_id_implENS1_11string_viewE _ZN4sycl3_V16detail18make_kernel_bundleEmRKNS0_7contextENS0_12bundle_stateENS0_7backendE _ZN4sycl3_V16detail18make_kernel_bundleEmRKNS0_7contextEbNS0_12bundle_stateENS0_7backendE _ZN4sycl3_V16detail18stringifyErrorCodeEi @@ -4130,7 +4130,7 @@ _ZN4sycl3_V17handler10depends_onERKSt6vectorINS0_5eventESaIS3_EE _ZN4sycl3_V17handler10mem_adviseEPKvmi _ZN4sycl3_V17handler10processArgEPvRKNS0_6detail19kernel_param_kind_tEimRmbb _ZN4sycl3_V17handler12addReductionERKSt10shared_ptrIKvE -_ZN4sycl3_V17handler13getKernelNameB5cxx11Ev +_ZN4sycl3_V17handler13getKernelNameEv _ZN4sycl3_V17handler14setNDRangeUsedEb _ZN4sycl3_V17handler15ext_oneapi_copyENS0_3ext6oneapi12experimental16image_mem_handleENS0_5rangeILi3EEERKNS4_16image_descriptorEPvS7_S7_S7_ _ZN4sycl3_V17handler15ext_oneapi_copyENS0_3ext6oneapi12experimental16image_mem_handleEPvRKNS4_16image_descriptorE @@ -4161,19 +4161,19 @@ _ZN4sycl3_V17handler22memcpyFromDeviceGlobalEPvPKvbmm _ZN4sycl3_V17handler22setHandlerKernelBundleENS0_6kernelE _ZN4sycl3_V17handler22setHandlerKernelBundleERKSt10shared_ptrINS0_6detail18kernel_bundle_implEE _ZN4sycl3_V17handler22setKernelIsCooperativeEb -_ZN4sycl3_V17handler22verifyUsedKernelBundleERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE _ZN4sycl3_V17handler24GetRangeRoundingSettingsERmS2_S2_ -_ZN4sycl3_V17handler24ext_intel_read_host_pipeERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEEPvmb +_ZN4sycl3_V17handler24ext_intel_read_host_pipeENS0_6detail11string_viewEPvmb _ZN4sycl3_V17handler24ext_oneapi_memcpy2d_implEPvmPKvmmm _ZN4sycl3_V17handler24ext_oneapi_memset2d_implEPvmimm _ZN4sycl3_V17handler24registerDynamicParameterERNS0_3ext6oneapi12experimental6detail22dynamic_parameter_baseEi -_ZN4sycl3_V17handler25ext_intel_write_host_pipeERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEEPvmb +_ZN4sycl3_V17handler25ext_intel_write_host_pipeENS0_6detail11string_viewEPvmb _ZN4sycl3_V17handler26associateWithHandlerCommonESt10shared_ptrINS0_6detail16AccessorImplHostEEi _ZN4sycl3_V17handler27computeFallbackKernelBoundsEmm _ZN4sycl3_V17handler28extractArgsAndReqsFromLambdaEPcmPKNS0_6detail19kernel_param_desc_tEb _ZN4sycl3_V17handler28memcpyToHostOnlyDeviceGlobalEPKvS3_mbmm _ZN4sycl3_V17handler28setStateExplicitKernelBundleEv _ZN4sycl3_V17handler30memcpyFromHostOnlyDeviceGlobalEPvPKvbmm +_ZN4sycl3_V17handler30verifyUsedKernelBundleInternalENS0_6detail11string_viewE _ZN4sycl3_V17handler34ext_oneapi_wait_external_semaphoreENS0_3ext6oneapi12experimental24interop_semaphore_handleE _ZN4sycl3_V17handler36ext_oneapi_signal_external_semaphoreENS0_3ext6oneapi12experimental24interop_semaphore_handleE _ZN4sycl3_V17handler6memcpyEPvPKvm @@ -4207,11 +4207,9 @@ _ZN4sycl3_V19exceptionC1ENS0_7contextEiRKNSt3_V214error_categoryEPKc _ZN4sycl3_V19exceptionC1ENS0_7contextEiRKNSt3_V214error_categoryERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE _ZN4sycl3_V19exceptionC1ESt10error_code _ZN4sycl3_V19exceptionC1ESt10error_codePKc -_ZN4sycl3_V19exceptionC1ESt10error_codeRKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE -_ZN4sycl3_V19exceptionC1ESt10error_codeSt10shared_ptrINS0_7contextEERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE +_ZN4sycl3_V19exceptionC1ESt10error_codeSt10shared_ptrINS0_7contextEEPKc _ZN4sycl3_V19exceptionC1EiRKNSt3_V214error_categoryE _ZN4sycl3_V19exceptionC1EiRKNSt3_V214error_categoryEPKc -_ZN4sycl3_V19exceptionC1EiRKNSt3_V214error_categoryERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE _ZN4sycl3_V19exceptionC2ENS0_7contextESt10error_code _ZN4sycl3_V19exceptionC2ENS0_7contextESt10error_codePKc _ZN4sycl3_V19exceptionC2ENS0_7contextESt10error_codeRKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE @@ -4220,11 +4218,9 @@ _ZN4sycl3_V19exceptionC2ENS0_7contextEiRKNSt3_V214error_categoryEPKc _ZN4sycl3_V19exceptionC2ENS0_7contextEiRKNSt3_V214error_categoryERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE _ZN4sycl3_V19exceptionC2ESt10error_code _ZN4sycl3_V19exceptionC2ESt10error_codePKc -_ZN4sycl3_V19exceptionC2ESt10error_codeRKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE -_ZN4sycl3_V19exceptionC2ESt10error_codeSt10shared_ptrINS0_7contextEERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE +_ZN4sycl3_V19exceptionC2ESt10error_codeSt10shared_ptrINS0_7contextEEPKc _ZN4sycl3_V19exceptionC2EiRKNSt3_V214error_categoryE _ZN4sycl3_V19exceptionC2EiRKNSt3_V214error_categoryEPKc -_ZN4sycl3_V19exceptionC2EiRKNSt3_V214error_categoryERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE _ZN4sycl3_V19exceptionD0Ev _ZN4sycl3_V19exceptionD1Ev _ZN4sycl3_V19exceptionD2Ev @@ -4489,6 +4485,144 @@ _ZNK4sycl3_V16detail30UnsampledImageAccessorBaseHost7getSizeEv _ZNK4sycl3_V16detail30UnsampledImageAccessorBaseHost8getPitchEv _ZNK4sycl3_V16device11get_backendEv _ZNK4sycl3_V16device12get_platformEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device10gpu_slicesEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device11free_memoryEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device11pci_addressEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device12gpu_eu_countEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device16memory_bus_widthEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device17gpu_eu_simd_widthEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device17max_mem_bandwidthEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device17memory_clock_rateEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device21gpu_hw_threads_per_euEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device23gpu_subslices_per_sliceEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device25gpu_eu_count_per_subsliceEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device25max_compute_queue_indicesEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device4uuidEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext5intel4info6device9device_idEEENS0_6detail11ABINeutralTINS8_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device12architectureEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device15max_work_groupsILi1EEEEENS0_6detail11ABINeutralTINSA_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device15max_work_groupsILi2EEEEENS0_6detail11ABINeutralTINSA_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device15max_work_groupsILi3EEEEENS0_6detail11ABINeutralTINSA_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device16composite_deviceEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device17component_devicesEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device19matrix_combinationsEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device21image_row_pitch_alignEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device21mipmap_max_anisotropyEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device22max_global_work_groupsEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device22max_image_linear_widthEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device23max_image_linear_heightEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext6oneapi12experimental4info6device26max_image_linear_row_pitchEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext8codeplay12experimental4info6device15supports_fusionEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_3ext8codeplay12experimental4info6device28max_registers_per_work_groupEEENS0_6detail11ABINeutralTINS9_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device10extensionsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device11device_typeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device12address_bitsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device12is_availableEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device12max_samplersEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device13image_supportEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device13parent_deviceEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device14driver_versionEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device14half_fp_configEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device14local_mem_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device14local_mem_typeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device15backend_versionEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device15ext_oneapi_srgbEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device15global_mem_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device15queue_profilingEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device15reference_countEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device15sub_group_sizesEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device16built_in_kernelsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device16double_fp_configEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device16is_endian_littleEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device16opencl_c_versionEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device16single_fp_configEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device17image2d_max_widthEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device17image3d_max_depthEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device17image3d_max_widthEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device17max_compute_unitsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device17max_constant_argsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device18image2d_max_heightEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device18image3d_max_heightEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device18max_mem_alloc_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device18max_num_sub_groupsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device18max_parameter_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device18printf_buffer_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device19built_in_kernel_idsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device19host_unified_memoryEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device19is_linker_availableEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device19max_clock_frequencyEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device19max_read_image_argsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device19max_work_group_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device19max_work_item_sizesILi1EEEEENS0_6detail11ABINeutralTINS7_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device19max_work_item_sizesILi2EEEEENS0_6detail11ABINeutralTINS7_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device19max_work_item_sizesILi3EEEEENS0_6detail11ABINeutralTINS7_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device19mem_base_addr_alignEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device20ext_intel_gpu_slicesEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device20image_max_array_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device20max_write_image_argsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device20partition_propertiesEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device20usm_host_allocationsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device21ext_intel_mem_channelEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device21ext_intel_pci_addressEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device21global_mem_cache_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device21global_mem_cache_typeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device21image_max_buffer_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device21is_compiler_availableEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device22execution_capabilitiesEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device22ext_intel_gpu_eu_countEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device22usm_device_allocationsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device22usm_shared_allocationsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device22usm_system_allocationsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device23native_vector_width_intEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device23partition_type_propertyEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device24error_correction_supportEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device24max_constant_buffer_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device24max_work_item_dimensionsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device24native_vector_width_charEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device24native_vector_width_halfEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device24native_vector_width_longEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device25native_vector_width_floatEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device25native_vector_width_shortEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device25partition_max_sub_devicesEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device26ext_intel_device_info_uuidEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device26global_mem_cache_line_sizeEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device26kernel_kernel_pipe_supportEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device26native_vector_width_doubleEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device26partition_affinity_domainsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device26preferred_vector_width_intEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device26profiling_timer_resolutionEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device27ext_intel_gpu_eu_simd_widthEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device27ext_intel_max_mem_bandwidthEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device27preferred_interop_user_syncEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device27preferred_vector_width_charEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device27preferred_vector_width_halfEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device27preferred_vector_width_longEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device28preferred_vector_width_floatEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device28preferred_vector_width_shortEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device29ext_oneapi_max_work_groups_1dEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device29ext_oneapi_max_work_groups_2dEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device29ext_oneapi_max_work_groups_3dEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device29preferred_vector_width_doubleEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device30partition_type_affinity_domainEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device31atomic_fence_order_capabilitiesEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device31atomic_fence_scope_capabilitiesEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device31ext_intel_gpu_hw_threads_per_euEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device32atomic_memory_order_capabilitiesEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device32atomic_memory_scope_capabilitiesEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device33ext_intel_gpu_subslices_per_sliceEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device33ext_oneapi_max_global_work_groupsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device33usm_restricted_shared_allocationsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device34ext_oneapi_bfloat16_math_functionsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device35ext_intel_gpu_eu_count_per_subsliceEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device38sub_group_independent_forward_progressEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device4nameEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device6vendorEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device7aspectsEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device7profileEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device7versionEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device8atomic64EEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device8platformEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16device13get_info_implINS0_4info6device9vendor_idEEENS0_6detail11ABINeutralTINS6_19is_device_info_descIT_E11return_typeEE4typeEv _ZNK4sycl3_V16device13has_extensionERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE _ZNK4sycl3_V16device14is_acceleratorEv _ZNK4sycl3_V16device18create_sub_devicesILNS0_4info18partition_propertyE4230EEESt6vectorIS1_SaIS1_EEm @@ -4503,148 +4637,15 @@ _ZNK4sycl3_V16device3hasENS0_6aspectE _ZNK4sycl3_V16device6is_cpuEv _ZNK4sycl3_V16device6is_gpuEv _ZNK4sycl3_V16device7is_hostEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device10gpu_slicesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device11free_memoryEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device11pci_addressEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device12gpu_eu_countEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device16memory_bus_widthEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device17gpu_eu_simd_widthEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device17max_mem_bandwidthEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device17memory_clock_rateEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device21gpu_hw_threads_per_euEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device23gpu_subslices_per_sliceEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device25gpu_eu_count_per_subsliceEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device25max_compute_queue_indicesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device4uuidEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext5intel4info6device9device_idEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device12architectureEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device15max_work_groupsILi1EEEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device15max_work_groupsILi2EEEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device15max_work_groupsILi3EEEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device16composite_deviceEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device17component_devicesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device19matrix_combinationsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device21image_row_pitch_alignEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device21mipmap_max_anisotropyEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device22max_global_work_groupsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device22max_image_linear_widthEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device23max_image_linear_heightEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext6oneapi12experimental4info6device26max_image_linear_row_pitchEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext8codeplay12experimental4info6device15supports_fusionEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_3ext8codeplay12experimental4info6device28max_registers_per_work_groupEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device10extensionsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device11device_typeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device12address_bitsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device12is_availableEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device12max_samplersEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device13image_supportEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device13parent_deviceEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device14driver_versionEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device14half_fp_configEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device14local_mem_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device14local_mem_typeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device15backend_versionEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device15ext_oneapi_srgbEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device15global_mem_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device15queue_profilingEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device15reference_countEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device15sub_group_sizesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device16built_in_kernelsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device16double_fp_configEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device16is_endian_littleEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device16opencl_c_versionEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device16single_fp_configEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device17image2d_max_widthEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device17image3d_max_depthEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device17image3d_max_widthEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device17max_compute_unitsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device17max_constant_argsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device18image2d_max_heightEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device18image3d_max_heightEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device18max_mem_alloc_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device18max_num_sub_groupsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device18max_parameter_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device18printf_buffer_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device19built_in_kernel_idsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device19host_unified_memoryEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device19is_linker_availableEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device19max_clock_frequencyEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device19max_read_image_argsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device19max_work_group_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device19max_work_item_sizesILi1EEEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device19max_work_item_sizesILi2EEEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device19max_work_item_sizesILi3EEEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device19mem_base_addr_alignEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device20ext_intel_gpu_slicesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device20image_max_array_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device20max_write_image_argsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device20partition_propertiesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device20usm_host_allocationsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device21ext_intel_mem_channelEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device21ext_intel_pci_addressEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device21global_mem_cache_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device21global_mem_cache_typeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device21image_max_buffer_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device21is_compiler_availableEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device22execution_capabilitiesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device22ext_intel_gpu_eu_countEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device22usm_device_allocationsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device22usm_shared_allocationsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device22usm_system_allocationsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device23native_vector_width_intEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device23partition_type_propertyEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device24error_correction_supportEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device24max_constant_buffer_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device24max_work_item_dimensionsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device24native_vector_width_charEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device24native_vector_width_halfEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device24native_vector_width_longEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device25native_vector_width_floatEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device25native_vector_width_shortEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device25partition_max_sub_devicesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device26ext_intel_device_info_uuidEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device26global_mem_cache_line_sizeEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device26kernel_kernel_pipe_supportEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device26native_vector_width_doubleEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device26partition_affinity_domainsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device26preferred_vector_width_intEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device26profiling_timer_resolutionEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device27ext_intel_gpu_eu_simd_widthEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device27ext_intel_max_mem_bandwidthEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device27preferred_interop_user_syncEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device27preferred_vector_width_charEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device27preferred_vector_width_halfEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device27preferred_vector_width_longEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device28preferred_vector_width_floatEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device28preferred_vector_width_shortEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device29ext_oneapi_max_work_groups_1dEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device29ext_oneapi_max_work_groups_2dEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device29ext_oneapi_max_work_groups_3dEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device29preferred_vector_width_doubleEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device30partition_type_affinity_domainEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device31atomic_fence_order_capabilitiesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device31atomic_fence_scope_capabilitiesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device31ext_intel_gpu_hw_threads_per_euEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device32atomic_memory_order_capabilitiesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device32atomic_memory_scope_capabilitiesEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device33ext_intel_gpu_subslices_per_sliceEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device33ext_oneapi_max_global_work_groupsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device33usm_restricted_shared_allocationsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device34ext_oneapi_bfloat16_math_functionsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device35ext_intel_gpu_eu_count_per_subsliceEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device38sub_group_independent_forward_progressEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device4nameEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device6vendorEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device7aspectsEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device7profileEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device7versionEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device8atomic64EEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device8platformEEENS0_6detail19is_device_info_descIT_E11return_typeEv -_ZNK4sycl3_V16device8get_infoINS0_4info6device9vendor_idEEENS0_6detail19is_device_info_descIT_E11return_typeEv _ZNK4sycl3_V16device9getNativeEv _ZNK4sycl3_V16kernel11get_backendEv _ZNK4sycl3_V16kernel11get_contextEv _ZNK4sycl3_V16kernel13getNativeImplEv +_ZNK4sycl3_V16kernel13get_info_implINS0_4info6kernel10attributesEEENS0_6detail11ABINeutralTINS6_19is_kernel_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16kernel13get_info_implINS0_4info6kernel13function_nameEEENS0_6detail11ABINeutralTINS6_19is_kernel_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16kernel13get_info_implINS0_4info6kernel15reference_countEEENS0_6detail11ABINeutralTINS6_19is_kernel_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16kernel13get_info_implINS0_4info6kernel7contextEEENS0_6detail11ABINeutralTINS6_19is_kernel_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V16kernel13get_info_implINS0_4info6kernel8num_argsEEENS0_6detail11ABINeutralTINS6_19is_kernel_info_descIT_E11return_typeEE4typeEv _ZNK4sycl3_V16kernel17get_kernel_bundleEv _ZNK4sycl3_V16kernel19ext_oneapi_get_infoINS0_3ext6oneapi12experimental4info21kernel_queue_specific23max_num_work_group_syncEEENT_11return_typeERKNS0_5queueE _ZNK4sycl3_V16kernel3getEv @@ -4660,11 +4661,6 @@ _ZNK4sycl3_V16kernel8get_infoINS0_4info22kernel_device_specific22compile_num_sub _ZNK4sycl3_V16kernel8get_infoINS0_4info22kernel_device_specific22compile_sub_group_sizeEEENS0_6detail35is_kernel_device_specific_info_descIT_E11return_typeERKNS0_6deviceE _ZNK4sycl3_V16kernel8get_infoINS0_4info22kernel_device_specific23compile_work_group_sizeEEENS0_6detail35is_kernel_device_specific_info_descIT_E11return_typeERKNS0_6deviceE _ZNK4sycl3_V16kernel8get_infoINS0_4info22kernel_device_specific34preferred_work_group_size_multipleEEENS0_6detail35is_kernel_device_specific_info_descIT_E11return_typeERKNS0_6deviceE -_ZNK4sycl3_V16kernel8get_infoINS0_4info6kernel10attributesEEENS0_6detail19is_kernel_info_descIT_E11return_typeEv -_ZNK4sycl3_V16kernel8get_infoINS0_4info6kernel13function_nameEEENS0_6detail19is_kernel_info_descIT_E11return_typeEv -_ZNK4sycl3_V16kernel8get_infoINS0_4info6kernel15reference_countEEENS0_6detail19is_kernel_info_descIT_E11return_typeEv -_ZNK4sycl3_V16kernel8get_infoINS0_4info6kernel7contextEEENS0_6detail19is_kernel_info_descIT_E11return_typeEv -_ZNK4sycl3_V16kernel8get_infoINS0_4info6kernel8num_argsEEENS0_6detail19is_kernel_info_descIT_E11return_typeEv _ZNK4sycl3_V16kernel9getNativeEv _ZNK4sycl3_V16stream12get_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEET_v _ZNK4sycl3_V16stream12get_propertyINS0_3ext6oneapi8property5queue12priority_lowEEET_v @@ -4798,17 +4794,17 @@ _ZNK4sycl3_V17samplereqERKS1_ _ZNK4sycl3_V17samplerneERKS1_ _ZNK4sycl3_V18platform11get_backendEv _ZNK4sycl3_V18platform11get_devicesENS0_4info11device_typeE +_ZNK4sycl3_V18platform13get_info_implINS0_4info8platform10extensionsEEENS0_6detail11ABINeutralTINS6_21is_platform_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V18platform13get_info_implINS0_4info8platform4nameEEENS0_6detail11ABINeutralTINS6_21is_platform_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V18platform13get_info_implINS0_4info8platform6vendorEEENS0_6detail11ABINeutralTINS6_21is_platform_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V18platform13get_info_implINS0_4info8platform7profileEEENS0_6detail11ABINeutralTINS6_21is_platform_info_descIT_E11return_typeEE4typeEv +_ZNK4sycl3_V18platform13get_info_implINS0_4info8platform7versionEEENS0_6detail11ABINeutralTINS6_21is_platform_info_descIT_E11return_typeEE4typeEv _ZNK4sycl3_V18platform13has_extensionERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE _ZNK4sycl3_V18platform30ext_oneapi_get_default_contextEv _ZNK4sycl3_V18platform32ext_oneapi_get_composite_devicesEv _ZNK4sycl3_V18platform3getEv _ZNK4sycl3_V18platform3hasENS0_6aspectE _ZNK4sycl3_V18platform7is_hostEv -_ZNK4sycl3_V18platform8get_infoINS0_4info8platform10extensionsEEENS0_6detail21is_platform_info_descIT_E11return_typeEv -_ZNK4sycl3_V18platform8get_infoINS0_4info8platform4nameEEENS0_6detail21is_platform_info_descIT_E11return_typeEv -_ZNK4sycl3_V18platform8get_infoINS0_4info8platform6vendorEEENS0_6detail21is_platform_info_descIT_E11return_typeEv -_ZNK4sycl3_V18platform8get_infoINS0_4info8platform7profileEEENS0_6detail21is_platform_info_descIT_E11return_typeEv -_ZNK4sycl3_V18platform8get_infoINS0_4info8platform7versionEEENS0_6detail21is_platform_info_descIT_E11return_typeEv _ZNK4sycl3_V18platform9getNativeEv _ZNK4sycl3_V19exception11get_cl_codeEv _ZNK4sycl3_V19exception11get_contextEv diff --git a/sycl/test/abi/symbol_size_alignment.cpp b/sycl/test/abi/symbol_size_alignment.cpp index fc9308d1682ca..04af22635b693 100644 --- a/sycl/test/abi/symbol_size_alignment.cpp +++ b/sycl/test/abi/symbol_size_alignment.cpp @@ -54,7 +54,7 @@ int main() { #ifdef _MSC_VER check(); #else - check(); + check(); #endif check, 16, 8>(); check(); diff --git a/sycl/unittests/program_manager/arg_mask/EliminatedArgMask.cpp b/sycl/unittests/program_manager/arg_mask/EliminatedArgMask.cpp index f9f580022ccad..35e353780d450 100644 --- a/sycl/unittests/program_manager/arg_mask/EliminatedArgMask.cpp +++ b/sycl/unittests/program_manager/arg_mask/EliminatedArgMask.cpp @@ -122,11 +122,7 @@ class MockHandler : public sycl::handler { std::move(CGH->MNDRDesc), std::move(CGH->MHostKernel), std::move(CGH->MKernel), std::move(MImpl->MKernelBundle), std::move(CGH->CGData), std::move(CGH->MArgs), -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES CGH->MKernelName.c_str(), std::move(CGH->MStreamStorage), -#else - std::move(CGH->MKernelName), std::move(CGH->MStreamStorage), -#endif std::move(MImpl->MAuxiliaryResources), CGH->MCGType, {}, MImpl->MKernelIsCooperative, CGH->MCodeLoc)); break; diff --git a/sycl/unittests/scheduler/SchedulerTestUtils.hpp b/sycl/unittests/scheduler/SchedulerTestUtils.hpp index 2a2f20c297a25..88ced1f25904a 100644 --- a/sycl/unittests/scheduler/SchedulerTestUtils.hpp +++ b/sycl/unittests/scheduler/SchedulerTestUtils.hpp @@ -258,11 +258,7 @@ class MockHandler : public sycl::handler { return CGData.MEvents; } std::vector &getArgs() { return MArgs; } -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES std::string getKernelName() { return MKernelName.c_str(); } -#else - std::string &getKernelName() { return MKernelName; } -#endif std::shared_ptr &getKernel() { return MKernel; } std::unique_ptr &getHostTask() { return MHostTask; } std::shared_ptr &getQueue() { return MQueue; }