From f70ad5bb25f5fa0fd8aa5d70dd0656c2a6d32a57 Mon Sep 17 00:00:00 2001 From: aelovikov-intel Date: Mon, 1 Apr 2024 13:05:20 -0700 Subject: [PATCH] [ABI-Break][SYCL] Enable "Neutral" ABI in regards to C++11 ABI by default (#13183) Co-authored-by: Alexey Bader --- sycl/include/sycl/detail/util.hpp | 8 +- 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 | 19 -- 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/layout_handler.cpp | 182 +++++----- sycl/test/abi/sycl_symbols_linux.dump | 314 +++++++++--------- sycl/test/abi/sycl_symbols_windows.dump | 304 ++++++++--------- sycl/test/abi/symbol_size_alignment.cpp | 4 +- .../arg_mask/EliminatedArgMask.cpp | 4 - .../scheduler/SchedulerTestUtils.hpp | 4 - 19 files changed, 394 insertions(+), 615 deletions(-) diff --git a/sycl/include/sycl/detail/util.hpp b/sycl/include/sycl/detail/util.hpp index 4b831e2e38e8f..d858aba279f41 100644 --- a/sycl/include/sycl/detail/util.hpp +++ b/sycl/include/sycl/detail/util.hpp @@ -11,9 +11,8 @@ #ifndef __SYCL_DEVICE_ONLY #include -#ifdef __INTEL_PREVIEW_BREAKING_CHANGES #include -#endif + #include #include #include @@ -69,7 +68,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 +83,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 a6968b481cd84..da5686a0818d2 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 /// Queries this SYCL device for SYCL backend-specific information. /// @@ -377,12 +368,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 353cde70e8bf9..fa4e5b6d7ba96 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 /// @@ -3414,17 +3403,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 @@ -3432,17 +3416,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 e92ca5441f9e0..ea491a28258df 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 /// Queries the kernel object for SYCL backend-specific information. /// @@ -201,12 +195,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 7e5919495dd60..6c8db5d4623c4 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,10 @@ 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 /// Queries this SYCL platform for SYCL backend-specific info. /// @@ -269,12 +252,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 dca210d8d1ffb..70aa37aad26a2 100644 --- a/sycl/source/device.cpp +++ b/sycl/source/device.cpp @@ -127,22 +127,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 @@ -157,11 +149,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 @@ -185,25 +173,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) @@ -211,15 +189,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 ff81752dc1f4e..ff14c0a879078 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 71bff195037a0..9434736a78dc7 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/layout_handler.cpp b/sycl/test/abi/layout_handler.cpp index 1bd3e2b9e48b8..444036971d9a7 100644 --- a/sycl/test/abi/layout_handler.cpp +++ b/sycl/test/abi/layout_handler.cpp @@ -33,7 +33,6 @@ void foo() { // CHECK-NEXT: 32 | struct std::_Vector_base, class std::allocator > > (base) // CHECK-NEXT: 32 | struct std::_Vector_base, class std::allocator > >::_Vector_impl _M_impl // CHECK-NEXT: 32 | class std::allocator > (base) (empty) -// CHECK-NEXT: 32 | class __gnu_cxx::new_allocator > (base) (empty) // CHECK: 32 | pointer _M_start // CHECK-NEXT: 40 | pointer _M_finish // CHECK-NEXT: 48 | pointer _M_end_of_storage @@ -41,7 +40,6 @@ void foo() { // CHECK-NEXT: 56 | struct std::_Vector_base, class std::allocator > > (base) // CHECK-NEXT: 56 | struct std::_Vector_base, class std::allocator > >::_Vector_impl _M_impl // CHECK-NEXT: 56 | class std::allocator > (base) (empty) -// CHECK-NEXT: 56 | class __gnu_cxx::new_allocator > (base) (empty) // CHECK: 56 | pointer _M_start // CHECK-NEXT: 64 | pointer _M_finish // CHECK-NEXT: 72 | pointer _M_end_of_storage @@ -49,7 +47,6 @@ void foo() { // CHECK-NEXT: 80 | struct std::_Vector_base, class std::allocator > > (base) // CHECK-NEXT: 80 | struct std::_Vector_base, class std::allocator > >::_Vector_impl _M_impl // CHECK-NEXT: 80 | class std::allocator > (base) (empty) -// CHECK-NEXT: 80 | class __gnu_cxx::new_allocator > (base) (empty) // CHECK: 80 | pointer _M_start // CHECK-NEXT: 88 | pointer _M_finish // CHECK-NEXT: 96 | pointer _M_end_of_storage @@ -57,7 +54,6 @@ void foo() { // CHECK-NEXT: 104 | struct std::_Vector_base > (base) // CHECK-NEXT: 104 | struct std::_Vector_base >::_Vector_impl _M_impl // CHECK-NEXT: 104 | class std::allocator (base) (empty) -// CHECK-NEXT: 104 | class __gnu_cxx::new_allocator (base) (empty) // CHECK: 104 | pointer _M_start // CHECK-NEXT: 112 | pointer _M_finish // CHECK-NEXT: 120 | pointer _M_end_of_storage @@ -65,7 +61,6 @@ void foo() { // CHECK-NEXT: 128 | struct std::_Vector_base, class std::allocator > > (base) // CHECK-NEXT: 128 | struct std::_Vector_base, class std::allocator > >::_Vector_impl _M_impl // CHECK-NEXT: 128 | class std::allocator > (base) (empty) -// CHECK-NEXT: 128 | class __gnu_cxx::new_allocator > (base) (empty) // CHECK: 128 | pointer _M_start // CHECK-NEXT: 136 | pointer _M_finish // CHECK-NEXT: 144 | pointer _M_end_of_storage @@ -73,7 +68,6 @@ void foo() { // CHECK-NEXT: 152 | struct std::_Vector_base, class std::allocator > > (base) // CHECK-NEXT: 152 | struct std::_Vector_base, class std::allocator > >::_Vector_impl _M_impl // CHECK-NEXT: 152 | class std::allocator > (base) (empty) -// CHECK-NEXT: 152 | class __gnu_cxx::new_allocator > (base) (empty) // CHECK: 152 | pointer _M_start // CHECK-NEXT: 160 | pointer _M_finish // CHECK-NEXT: 168 | pointer _M_end_of_storage @@ -81,7 +75,6 @@ void foo() { // CHECK-NEXT: 176 | struct std::_Vector_base, class std::allocator > > (base) // CHECK-NEXT: 176 | struct std::_Vector_base, class std::allocator > >::_Vector_impl _M_impl // CHECK-NEXT: 176 | class std::allocator > (base) (empty) -// CHECK-NEXT: 176 | class __gnu_cxx::new_allocator > (base) (empty) // CHECK: 176 | pointer _M_start // CHECK-NEXT: 184 | pointer _M_finish // CHECK-NEXT: 192 | pointer _M_end_of_storage @@ -89,7 +82,6 @@ void foo() { // CHECK-NEXT: 200 | struct std::_Vector_base > (base) // CHECK-NEXT: 200 | struct std::_Vector_base >::_Vector_impl _M_impl // CHECK-NEXT: 200 | class std::allocator (base) (empty) -// CHECK-NEXT: 200 | class __gnu_cxx::new_allocator (base) (empty) // CHECK: 200 | pointer _M_start // CHECK-NEXT: 208 | pointer _M_finish // CHECK-NEXT: 216 | pointer _M_end_of_storage @@ -97,7 +89,6 @@ void foo() { // CHECK-NEXT: 224 | struct std::_Vector_base > (base) // CHECK-NEXT: 224 | struct std::_Vector_base >::_Vector_impl _M_impl // CHECK-NEXT: 224 | class std::allocator (base) (empty) -// CHECK-NEXT: 224 | class __gnu_cxx::new_allocator (base) (empty) // CHECK: 224 | pointer _M_start // CHECK-NEXT: 232 | pointer _M_finish // CHECK-NEXT: 240 | pointer _M_end_of_storage @@ -115,94 +106,85 @@ void foo() { // CHECK-NEXT: 320 | class sycl::detail::array<3> (base) // CHECK-NEXT: 320 | size_t[3] common_array // CHECK-NEXT: 344 | size_t Dims -// CHECK-NEXT: 352 | class std::basic_string MKernelName -// CHECK-NEXT: 352 | struct std::basic_string::_Alloc_hider _M_dataplus -// CHECK-NEXT: 352 | class std::allocator (base) (empty) -// CHECK-NEXT: 352 | class __gnu_cxx::new_allocator (base) (empty) -// CHECK-NEXT: 352 | pointer _M_p -// CHECK-NEXT: 360 | size_type _M_string_length -// CHECK-NEXT: 368 | union std::basic_string::(anonymous at {{.*}}) -// CHECK-NEXT: 368 | char[16] _M_local_buf -// CHECK-NEXT: 368 | size_type _M_allocated_capacity -// CHECK-NEXT: 384 | class std::shared_ptr MKernel -// CHECK-NEXT: 384 | class std::__shared_ptr (base) -// CHECK-NEXT: 384 | class std::__shared_ptr_access (base) (empty) -// CHECK-NEXT: 384 | element_type * _M_ptr -// CHECK-NEXT: 392 | class std::__shared_count<> _M_refcount -// CHECK-NEXT: 392 | _Sp_counted_base<(_Lock_policy)2U> * _M_pi -// CHECK-NEXT: 400 | detail::class CG::CGTYPE MCGType -// CHECK-NEXT: 408 | void * MSrcPtr -// CHECK-NEXT: 416 | void * MDstPtr -// CHECK-NEXT: 424 | size_t MLength -// CHECK-NEXT: 432 | class std::vector MPattern -// CHECK-NEXT: 432 | struct std::_Vector_base > (base) -// CHECK-NEXT: 432 | struct std::_Vector_base >::_Vector_impl _M_impl -// CHECK-NEXT: 432 | class std::allocator (base) (empty) -// CHECK-NEXT: 432 | class __gnu_cxx::new_allocator (base) (empty) -// CHECK: 432 | pointer _M_start -// CHECK-NEXT: 440 | pointer _M_finish -// CHECK-NEXT: 448 | pointer _M_end_of_storage -// CHECK-NEXT: 456 | class std::unique_ptr MHostKernel -// CHECK: 456 | class std::__uniq_ptr_impl > -// CHECK-NEXT: 456 | class std::tuple > _M_t -// CHECK-NEXT: 456 | struct std::_Tuple_impl<0, class sycl::detail::HostKernelBase *, struct std::default_delete > (base) -// CHECK-NEXT: 456 | struct std::_Tuple_impl<1, struct std::default_delete > (base) (empty) -// CHECK: 456 | struct std::_Head_base<0, class sycl::detail::HostKernelBase *> (base) -// CHECK-NEXT: 456 | class sycl::detail::HostKernelBase * _M_head_impl -// CHECK-NEXT: 464 | class std::unique_ptr MHostTask -// CHECK: 464 | class std::__uniq_ptr_impl > -// CHECK-NEXT: 464 | class std::tuple > _M_t -// CHECK-NEXT: 464 | struct std::_Tuple_impl<0, class sycl::detail::HostTask *, struct std::default_delete > (base) -// CHECK-NEXT: 464 | struct std::_Tuple_impl<1, struct std::default_delete > (base) (empty) -// CHECK: 464 | struct std::_Head_base<0, class sycl::detail::HostTask *> (base) -// CHECK-NEXT: 464 | class sycl::detail::HostTask * _M_head_impl -// CHECK-NEXT: 472 | class std::vector > MEventsWaitWithBarrier -// CHECK-NEXT: 472 | struct std::_Vector_base, class std::allocator > > (base) -// CHECK-NEXT: 472 | struct std::_Vector_base, class std::allocator > >::_Vector_impl _M_impl -// CHECK-NEXT: 472 | class std::allocator > (base) (empty) -// CHECK-NEXT: 472 | class __gnu_cxx::new_allocator > (base) (empty) -// CHECK: 472 | pointer _M_start -// CHECK-NEXT: 480 | pointer _M_finish -// CHECK-NEXT: 488 | pointer _M_end_of_storage -// CHECK-NEXT: 496 | class std::shared_ptr MGraph -// CHECK-NEXT: 496 | class std::__shared_ptr (base) -// CHECK-NEXT: 496 | class std::__shared_ptr_access (base) (empty) -// CHECK-NEXT: 496 | element_type * _M_ptr -// CHECK-NEXT: 504 | class std::__shared_count<> _M_refcount -// CHECK-NEXT: 504 | _Sp_counted_base<(_Lock_policy)2U> * _M_pi -// CHECK-NEXT: 512 | class std::shared_ptr MExecGraph -// CHECK-NEXT: 512 | class std::__shared_ptr (base) -// CHECK-NEXT: 512 | class std::__shared_ptr_access (base) (empty) -// CHECK-NEXT: 512 | element_type * _M_ptr -// CHECK-NEXT: 520 | class std::__shared_count<> _M_refcount -// CHECK-NEXT: 520 | _Sp_counted_base<(_Lock_policy)2U> * _M_pi -// CHECK-NEXT: 528 | class std::shared_ptr MSubgraphNode -// CHECK-NEXT: 528 | class std::__shared_ptr (base) -// CHECK-NEXT: 528 | class std::__shared_ptr_access (base) (empty) -// CHECK-NEXT: 528 | element_type * _M_ptr -// CHECK-NEXT: 536 | class std::__shared_count<> _M_refcount -// CHECK-NEXT: 536 | _Sp_counted_base<(_Lock_policy)2U> * _M_pi -// CHECK-NEXT: 544 | class std::unique_ptr MGraphNodeCG -// CHECK: 544 | class std::__uniq_ptr_impl > -// CHECK-NEXT: 544 | class std::tuple > _M_t -// CHECK-NEXT: 544 | struct std::_Tuple_impl<0, class sycl::detail::CG *, struct std::default_delete > (base) -// CHECK-NEXT: 544 | struct std::_Tuple_impl<1, struct std::default_delete > (base) (empty) -// CHECK: 544 | struct std::_Head_base<0, class sycl::detail::CG *> (base) -// CHECK-NEXT: 544 | class sycl::detail::CG * _M_head_impl -// CHECK-NEXT: 552 | _Bool MIsHost -// CHECK-NEXT: 560 | struct sycl::detail::code_location MCodeLoc -// CHECK-NEXT: 560 | const char * MFileName -// CHECK-NEXT: 568 | const char * MFunctionName -// CHECK-NEXT: 576 | unsigned long MLineNo -// CHECK-NEXT: 584 | unsigned long MColumnNo -// CHECK-NEXT: 592 | _Bool MIsFinalized -// CHECK-NEXT: 600 | class sycl::event MLastEvent -// CHECK-NEXT: 600 | class sycl::detail::OwnerLessBase (base) (empty) -// CHECK-NEXT: 600 | class std::shared_ptr impl -// CHECK-NEXT: 600 | class std::__shared_ptr (base) -// CHECK-NEXT: 600 | class std::__shared_ptr_access (base) (empty) -// CHECK-NEXT: 600 | element_type * _M_ptr -// CHECK-NEXT: 608 | class std::__shared_count<> _M_refcount -// CHECK-NEXT: 608 | _Sp_counted_base<(_Lock_policy)2U> * _M_pi -// CHECK-NEXT: | [sizeof=616, dsize=616, align=8, -// CHECK-NEXT: | nvsize=616, nvalign=8] +// CHECK-NEXT: 352 | class sycl::detail::string MKernelName +// CHECK-NEXT: 352 | char * str +// CHECK-NEXT: 360 | class std::shared_ptr MKernel +// CHECK-NEXT: 360 | class std::__shared_ptr (base) +// CHECK-NEXT: 360 | class std::__shared_ptr_access (base) (empty) +// CHECK-NEXT: 360 | element_type * _M_ptr +// CHECK-NEXT: 368 | class std::__shared_count<> _M_refcount +// CHECK-NEXT: 368 | _Sp_counted_base<(_Lock_policy)2U> * _M_pi +// CHECK-NEXT: 376 | detail::class CG::CGTYPE MCGType +// CHECK-NEXT: 384 | void * MSrcPtr +// CHECK-NEXT: 392 | void * MDstPtr +// CHECK-NEXT: 400 | size_t MLength +// CHECK-NEXT: 408 | class std::vector MPattern +// CHECK-NEXT: 408 | struct std::_Vector_base > (base) +// CHECK-NEXT: 408 | struct std::_Vector_base >::_Vector_impl _M_impl +// CHECK-NEXT: 408 | class std::allocator (base) (empty) +// CHECK: 408 | pointer _M_start +// CHECK-NEXT: 416 | pointer _M_finish +// CHECK-NEXT: 424 | pointer _M_end_of_storage +// CHECK-NEXT: 432 | class std::unique_ptr MHostKernel +// CHECK: 432 | class std::__uniq_ptr_impl > (base) +// CHECK-NEXT: 432 | class std::tuple > _M_t +// CHECK-NEXT: 432 | struct std::_Tuple_impl<0, class sycl::detail::HostKernelBase *, struct std::default_delete > (base) +// CHECK-NEXT: 432 | struct std::_Tuple_impl<1, struct std::default_delete > (base) (empty) +// CHECK: 432 | struct std::_Head_base<0, class sycl::detail::HostKernelBase *> (base) +// CHECK-NEXT: 432 | class sycl::detail::HostKernelBase * _M_head_impl +// CHECK-NEXT: 440 | class std::unique_ptr MHostTask +// CHECK: 440 | class std::__uniq_ptr_impl > (base) +// CHECK-NEXT: 440 | class std::tuple > _M_t +// CHECK-NEXT: 440 | struct std::_Tuple_impl<0, class sycl::detail::HostTask *, struct std::default_delete > (base) +// CHECK-NEXT: 440 | struct std::_Tuple_impl<1, struct std::default_delete > (base) (empty) +// CHECK: 440 | struct std::_Head_base<0, class sycl::detail::HostTask *> (base) +// CHECK-NEXT: 440 | class sycl::detail::HostTask * _M_head_impl +// CHECK-NEXT: 448 | class std::vector > MEventsWaitWithBarrier +// CHECK-NEXT: 448 | struct std::_Vector_base, class std::allocator > > (base) +// CHECK-NEXT: 448 | struct std::_Vector_base, class std::allocator > >::_Vector_impl _M_impl +// CHECK-NEXT: 448 | class std::allocator > (base) (empty) +// CHECK: 448 | pointer _M_start +// CHECK-NEXT: 456 | pointer _M_finish +// CHECK-NEXT: 464 | pointer _M_end_of_storage +// CHECK-NEXT: 472 | class std::shared_ptr MGraph +// CHECK-NEXT: 472 | class std::__shared_ptr (base) +// CHECK-NEXT: 472 | class std::__shared_ptr_access (base) (empty) +// CHECK-NEXT: 472 | element_type * _M_ptr +// CHECK-NEXT: 480 | class std::__shared_count<> _M_refcount +// CHECK-NEXT: 480 | _Sp_counted_base<(_Lock_policy)2U> * _M_pi +// CHECK-NEXT: 488 | class std::shared_ptr MExecGraph +// CHECK-NEXT: 488 | class std::__shared_ptr (base) +// CHECK-NEXT: 488 | class std::__shared_ptr_access (base) (empty) +// CHECK-NEXT: 488 | element_type * _M_ptr +// CHECK-NEXT: 496 | class std::__shared_count<> _M_refcount +// CHECK-NEXT: 496 | _Sp_counted_base<(_Lock_policy)2U> * _M_pi +// CHECK-NEXT: 504 | class std::shared_ptr MSubgraphNode +// CHECK-NEXT: 504 | class std::__shared_ptr (base) +// CHECK-NEXT: 504 | class std::__shared_ptr_access (base) (empty) +// CHECK-NEXT: 504 | element_type * _M_ptr +// CHECK-NEXT: 512 | class std::__shared_count<> _M_refcount +// CHECK-NEXT: 512 | _Sp_counted_base<(_Lock_policy)2U> * _M_pi +// CHECK-NEXT: 520 | class std::unique_ptr MGraphNodeCG +// CHECK: 520 | class std::__uniq_ptr_impl > (base) +// CHECK-NEXT: 520 | class std::tuple > _M_t +// CHECK-NEXT: 520 | struct std::_Tuple_impl<0, class sycl::detail::CG *, struct std::default_delete > (base) +// CHECK-NEXT: 520 | struct std::_Tuple_impl<1, struct std::default_delete > (base) (empty) +// CHECK: 520 | struct std::_Head_base<0, class sycl::detail::CG *> (base) +// CHECK-NEXT: 520 | class sycl::detail::CG * _M_head_impl +// CHECK-NEXT: 528 | _Bool MIsHost +// CHECK-NEXT: 536 | struct sycl::detail::code_location MCodeLoc +// CHECK-NEXT: 536 | const char * MFileName +// CHECK-NEXT: 544 | const char * MFunctionName +// CHECK-NEXT: 552 | unsigned long MLineNo +// CHECK-NEXT: 560 | unsigned long MColumnNo +// CHECK-NEXT: 568 | _Bool MIsFinalized +// CHECK-NEXT: 576 | class sycl::event MLastEvent +// CHECK-NEXT: 576 | class sycl::detail::OwnerLessBase (base) (empty) +// CHECK-NEXT: 576 | class std::shared_ptr impl +// CHECK-NEXT: 576 | class std::__shared_ptr (base) +// CHECK-NEXT: 576 | class std::__shared_ptr_access (base) (empty) +// CHECK-NEXT: 576 | element_type * _M_ptr +// CHECK-NEXT: 584 | class std::__shared_count<> _M_refcount +// CHECK-NEXT: 584 | _Sp_counted_base<(_Lock_policy)2U> * _M_pi +// CHECK-NEXT: | [sizeof=592, dsize=592, align=8, +// CHECK-NEXT: | nvsize=592, nvalign=8] diff --git a/sycl/test/abi/sycl_symbols_linux.dump b/sycl/test/abi/sycl_symbols_linux.dump index f46e5a17480fc..9f46f7369dfdb 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 @@ -4495,6 +4491,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_V16device16get_backend_infoINS0_4info6device15backend_versionEEENS0_6detail20is_backend_info_descIT_E11return_typeEv @@ -4512,144 +4646,6 @@ _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 @@ -4657,6 +4653,11 @@ _ZNK4sycl3_V16kernel13getNativeImplEv _ZNK4sycl3_V16kernel16get_backend_infoINS0_4info6device15backend_versionEEENS0_6detail20is_backend_info_descIT_E11return_typeEv _ZNK4sycl3_V16kernel16get_backend_infoINS0_4info6device7versionEEENS0_6detail20is_backend_info_descIT_E11return_typeEv _ZNK4sycl3_V16kernel16get_backend_infoINS0_4info8platform7versionEEENS0_6detail20is_backend_info_descIT_E11return_typeEv +_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 @@ -4672,11 +4673,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 @@ -4813,6 +4809,11 @@ _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_V18platform16get_backend_infoINS0_4info6device15backend_versionEEENS0_6detail20is_backend_info_descIT_E11return_typeEv _ZNK4sycl3_V18platform16get_backend_infoINS0_4info6device7versionEEENS0_6detail20is_backend_info_descIT_E11return_typeEv @@ -4822,11 +4823,6 @@ _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/sycl_symbols_windows.dump b/sycl/test/abi/sycl_symbols_windows.dump index 69076eaf8d775..f956e1acf988a 100644 --- a/sycl/test/abi/sycl_symbols_windows.dump +++ b/sycl/test/abi/sycl_symbols_windows.dump @@ -38,206 +38,206 @@ ??$get_backend_info@Uversion@platform@info@_V1@sycl@@@kernel@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ ??$get_backend_info@Uversion@platform@info@_V1@sycl@@@platform@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ ??$get_backend_info@Uversion@platform@info@_V1@sycl@@@queue@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@U?$max_work_groups@$00@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$id@$00@12@XZ ??$get_info@U?$max_work_groups@$00@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA?AV?$id@$00@23@XZ -??$get_info@U?$max_work_groups@$01@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$id@$01@12@XZ ??$get_info@U?$max_work_groups@$01@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA?AV?$id@$01@23@XZ -??$get_info@U?$max_work_groups@$02@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$id@$02@12@XZ ??$get_info@U?$max_work_groups@$02@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA?AV?$id@$02@23@XZ -??$get_info@U?$max_work_item_sizes@$00@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$range@$00@12@XZ -??$get_info@U?$max_work_item_sizes@$01@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$range@$01@12@XZ -??$get_info@U?$max_work_item_sizes@$02@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$range@$02@12@XZ -??$get_info@Uaddress_bits@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Uarchitecture@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBA?AW4architecture@experimental@oneapi@ext@12@XZ ??$get_info@Uarchitecture@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA?AW4architecture@experimental@oneapi@ext@23@XZ -??$get_info@Uaspects@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4aspect@_V1@sycl@@V?$allocator@W4aspect@_V1@sycl@@@std@@@std@@XZ -??$get_info@Uatomic64@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ ??$get_info@Uatomic_fence_order_capabilities@context@info@_V1@sycl@@@context@_V1@sycl@@QEBA?AV?$vector@W4memory_order@_V1@sycl@@V?$allocator@W4memory_order@_V1@sycl@@@std@@@std@@XZ -??$get_info@Uatomic_fence_order_capabilities@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4memory_order@_V1@sycl@@V?$allocator@W4memory_order@_V1@sycl@@@std@@@std@@XZ ??$get_info@Uatomic_fence_scope_capabilities@context@info@_V1@sycl@@@context@_V1@sycl@@QEBA?AV?$vector@W4memory_scope@_V1@sycl@@V?$allocator@W4memory_scope@_V1@sycl@@@std@@@std@@XZ -??$get_info@Uatomic_fence_scope_capabilities@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4memory_scope@_V1@sycl@@V?$allocator@W4memory_scope@_V1@sycl@@@std@@@std@@XZ ??$get_info@Uatomic_memory_order_capabilities@context@info@_V1@sycl@@@context@_V1@sycl@@QEBA?AV?$vector@W4memory_order@_V1@sycl@@V?$allocator@W4memory_order@_V1@sycl@@@std@@@std@@XZ -??$get_info@Uatomic_memory_order_capabilities@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4memory_order@_V1@sycl@@V?$allocator@W4memory_order@_V1@sycl@@@std@@@std@@XZ ??$get_info@Uatomic_memory_scope_capabilities@context@info@_V1@sycl@@@context@_V1@sycl@@QEBA?AV?$vector@W4memory_scope@_V1@sycl@@V?$allocator@W4memory_scope@_V1@sycl@@@std@@@std@@XZ -??$get_info@Uatomic_memory_scope_capabilities@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4memory_scope@_V1@sycl@@V?$allocator@W4memory_scope@_V1@sycl@@@std@@@std@@XZ -??$get_info@Uattributes@kernel@info@_V1@sycl@@@kernel@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Ubackend_version@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Ubuilt_in_kernel_ids@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@Vkernel_id@_V1@sycl@@V?$allocator@Vkernel_id@_V1@sycl@@@std@@@std@@XZ -??$get_info@Ubuilt_in_kernels@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@V?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@V?$allocator@V?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@@2@@std@@XZ ??$get_info@Ucommand_execution_status@event@info@_V1@sycl@@@event@_V1@sycl@@QEBA?AW4event_command_status@info@12@XZ ??$get_info@Ucompile_num_sub_groups@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBAIAEBVdevice@12@@Z ??$get_info@Ucompile_sub_group_size@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBAIAEBVdevice@12@@Z ??$get_info@Ucompile_work_group_size@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBA?AV?$range@$02@12@AEBVdevice@12@@Z -??$get_info@Ucomponent_devices@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@Vdevice@_V1@sycl@@V?$allocator@Vdevice@_V1@sycl@@@std@@@std@@XZ ??$get_info@Ucomponent_devices@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA?AV?$vector@Vdevice@_V1@sycl@@V?$allocator@Vdevice@_V1@sycl@@@std@@@std@@XZ -??$get_info@Ucomposite_device@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBA?AV012@XZ ??$get_info@Ucomposite_device@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA?AVdevice@23@XZ -??$get_info@Ucontext@kernel@info@_V1@sycl@@@kernel@_V1@sycl@@QEBA?AVcontext@12@XZ ??$get_info@Ucontext@queue@info@_V1@sycl@@@queue@_V1@sycl@@QEBA?AVcontext@12@XZ ??$get_info@Udevice@queue@info@_V1@sycl@@@queue@_V1@sycl@@QEBA?AVdevice@12@XZ -??$get_info@Udevice_id@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Udevice_id@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Udevice_type@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AW4device_type@info@12@XZ ??$get_info@Udevices@context@info@_V1@sycl@@@context@_V1@sycl@@QEBA?AV?$vector@Vdevice@_V1@sycl@@V?$allocator@Vdevice@_V1@sycl@@@std@@@std@@XZ -??$get_info@Udouble_fp_config@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4fp_config@info@_V1@sycl@@V?$allocator@W4fp_config@info@_V1@sycl@@@std@@@std@@XZ -??$get_info@Udriver_version@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Uerror_correction_support@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uexecution_capabilities@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4execution_capability@info@_V1@sycl@@V?$allocator@W4execution_capability@info@_V1@sycl@@@std@@@std@@XZ ??$get_info@Uext_codeplay_num_regs@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBAIAEBVdevice@12@@Z -??$get_info@Uext_intel_device_info_uuid@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$array@E$0BA@@std@@XZ -??$get_info@Uext_intel_gpu_eu_count@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Uext_intel_gpu_eu_count_per_subslice@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Uext_intel_gpu_eu_simd_width@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Uext_intel_gpu_hw_threads_per_eu@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Uext_intel_gpu_slices@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Uext_intel_gpu_subslices_per_slice@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Uext_intel_max_mem_bandwidth@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uext_intel_mem_channel@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uext_intel_pci_address@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Uext_oneapi_bfloat16_math_functions@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uext_oneapi_max_global_work_groups@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uext_oneapi_max_work_groups_1d@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$id@$00@12@XZ -??$get_info@Uext_oneapi_max_work_groups_2d@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$id@$01@12@XZ -??$get_info@Uext_oneapi_max_work_groups_3d@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$id@$02@12@XZ -??$get_info@Uext_oneapi_srgb@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uextensions@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@V?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@V?$allocator@V?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@@2@@std@@XZ -??$get_info@Uextensions@platform@info@_V1@sycl@@@platform@_V1@sycl@@QEBA?AV?$vector@V?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@V?$allocator@V?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@@2@@std@@XZ -??$get_info@Ufree_memory@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ ??$get_info@Ufree_memory@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA_KXZ -??$get_info@Ufunction_name@kernel@info@_V1@sycl@@@kernel@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Uglobal_mem_cache_line_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Uglobal_mem_cache_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uglobal_mem_cache_type@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AW4global_mem_cache_type@info@12@XZ -??$get_info@Uglobal_mem_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ ??$get_info@Uglobal_work_size@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBA?AV?$range@$02@12@AEBVdevice@12@@Z -??$get_info@Ugpu_eu_count@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Ugpu_eu_count@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Ugpu_eu_count_per_subslice@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Ugpu_eu_count_per_subslice@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Ugpu_eu_simd_width@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Ugpu_eu_simd_width@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Ugpu_hw_threads_per_eu@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Ugpu_hw_threads_per_eu@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Ugpu_slices@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Ugpu_slices@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Ugpu_subslices_per_slice@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Ugpu_subslices_per_slice@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Uhalf_fp_config@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4fp_config@info@_V1@sycl@@V?$allocator@W4fp_config@info@_V1@sycl@@@std@@@std@@XZ -??$get_info@Uhost_unified_memory@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uimage2d_max_height@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uimage2d_max_width@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uimage3d_max_depth@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uimage3d_max_height@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uimage3d_max_width@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uimage_max_array_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uimage_max_buffer_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uimage_row_pitch_align@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Uimage_row_pitch_align@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Uimage_support@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uis_available@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uis_compiler_available@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uis_endian_little@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uis_linker_available@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Ukernel_kernel_pipe_support@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Ulocal_mem_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Ulocal_mem_type@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AW4local_mem_type@info@12@XZ -??$get_info@Umatrix_combinations@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@Ucombination@matrix@experimental@oneapi@ext@_V1@sycl@@V?$allocator@Ucombination@matrix@experimental@oneapi@ext@_V1@sycl@@@std@@@std@@XZ ??$get_info@Umatrix_combinations@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA?AV?$vector@Ucombination@matrix@experimental@oneapi@ext@_V1@sycl@@V?$allocator@Ucombination@matrix@experimental@oneapi@ext@_V1@sycl@@@std@@@std@@XZ -??$get_info@Umax_clock_frequency@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Umax_compute_queue_indices@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBAHXZ ??$get_info@Umax_compute_queue_indices@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAHXZ -??$get_info@Umax_compute_units@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Umax_constant_args@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Umax_constant_buffer_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Umax_global_work_groups@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ ??$get_info@Umax_global_work_groups@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA_KXZ -??$get_info@Umax_image_linear_height@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Umax_image_linear_height@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Umax_image_linear_row_pitch@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Umax_image_linear_row_pitch@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Umax_image_linear_width@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Umax_image_linear_width@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Umax_mem_alloc_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Umax_mem_bandwidth@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ ??$get_info@Umax_mem_bandwidth@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA_KXZ -??$get_info@Umax_num_sub_groups@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Umax_num_sub_groups@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBAIAEBVdevice@12@@Z -??$get_info@Umax_parameter_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Umax_read_image_args@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Umax_registers_per_work_group@device@info@experimental@codeplay@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Umax_registers_per_work_group@device@info@experimental@codeplay@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Umax_samplers@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Umax_sub_group_size@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBAIAEBVdevice@12@@Z ??$get_info@Umax_sub_group_size@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBAIAEBVdevice@12@AEBV?$range@$02@12@@Z -??$get_info@Umax_work_group_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Umax_work_item_dimensions@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Umax_write_image_args@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Umem_base_addr_align@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Umemory_bus_width@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Umemory_bus_width@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Umemory_clock_rate@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Umemory_clock_rate@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAIXZ -??$get_info@Umipmap_max_anisotropy@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@QEBAMXZ ??$get_info@Umipmap_max_anisotropy@device@info@experimental@oneapi@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBAMXZ -??$get_info@Uname@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Uname@platform@info@_V1@sycl@@@platform@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Unative_vector_width_char@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Unative_vector_width_double@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Unative_vector_width_float@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Unative_vector_width_half@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Unative_vector_width_int@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Unative_vector_width_long@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Unative_vector_width_short@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Unum_args@kernel@info@_V1@sycl@@@kernel@_V1@sycl@@QEBAIXZ -??$get_info@Uopencl_c_version@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Uparent_device@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV012@XZ -??$get_info@Upartition_affinity_domains@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4partition_affinity_domain@info@_V1@sycl@@V?$allocator@W4partition_affinity_domain@info@_V1@sycl@@@std@@@std@@XZ -??$get_info@Upartition_max_sub_devices@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Upartition_properties@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4partition_property@info@_V1@sycl@@V?$allocator@W4partition_property@info@_V1@sycl@@@std@@@std@@XZ -??$get_info@Upartition_type_affinity_domain@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AW4partition_affinity_domain@info@12@XZ -??$get_info@Upartition_type_property@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AW4partition_property@info@12@XZ -??$get_info@Upci_address@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ ??$get_info@Upci_address@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ ??$get_info@Uplatform@context@info@_V1@sycl@@@context@_V1@sycl@@QEBA?AVplatform@12@XZ -??$get_info@Uplatform@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AVplatform@12@XZ -??$get_info@Upreferred_interop_user_sync@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Upreferred_vector_width_char@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Upreferred_vector_width_double@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Upreferred_vector_width_float@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Upreferred_vector_width_half@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Upreferred_vector_width_int@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Upreferred_vector_width_long@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Upreferred_vector_width_short@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Upreferred_work_group_size_multiple@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBA_KAEBVdevice@12@@Z -??$get_info@Uprintf_buffer_size@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ ??$get_info@Uprivate_mem_size@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBA_KAEBVdevice@12@@Z -??$get_info@Uprofile@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Uprofile@platform@info@_V1@sycl@@@platform@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Uprofiling_timer_resolution@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_KXZ -??$get_info@Uqueue_profiling@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ ??$get_info@Ureference_count@context@info@_V1@sycl@@@context@_V1@sycl@@QEBAIXZ -??$get_info@Ureference_count@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ ??$get_info@Ureference_count@event@info@_V1@sycl@@@event@_V1@sycl@@QEBAIXZ -??$get_info@Ureference_count@kernel@info@_V1@sycl@@@kernel@_V1@sycl@@QEBAIXZ ??$get_info@Ureference_count@queue@info@_V1@sycl@@@queue@_V1@sycl@@QEBAIXZ -??$get_info@Usingle_fp_config@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@W4fp_config@info@_V1@sycl@@V?$allocator@W4fp_config@info@_V1@sycl@@@std@@@std@@XZ -??$get_info@Usub_group_independent_forward_progress@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Usub_group_sizes@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$vector@_KV?$allocator@_K@std@@@std@@XZ -??$get_info@Usupports_fusion@device@info@experimental@codeplay@ext@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ ??$get_info@Usupports_fusion@device@info@experimental@codeplay@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA_NXZ -??$get_info@Uusm_device_allocations@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uusm_host_allocations@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uusm_restricted_shared_allocations@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uusm_shared_allocations@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uusm_system_allocations@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA_NXZ -??$get_info@Uuuid@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$array@E$0BA@@std@@XZ ??$get_info@Uuuid@device@info@intel@ext@_V1@sycl@@@device_impl@detail@_V1@sycl@@QEBA?AV?$array@E$0BA@@std@@XZ -??$get_info@Uvendor@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Uvendor@platform@info@_V1@sycl@@@platform@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Uvendor_id@device@info@_V1@sycl@@@device@_V1@sycl@@QEBAIXZ -??$get_info@Uversion@device@info@_V1@sycl@@@device@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ -??$get_info@Uversion@platform@info@_V1@sycl@@@platform@_V1@sycl@@QEBA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ ??$get_info@Uwork_group_size@kernel_device_specific@info@_V1@sycl@@@kernel@_V1@sycl@@QEBA_KAEBVdevice@12@@Z +??$get_info_impl@U?$max_work_groups@$00@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$id@$00@12@XZ +??$get_info_impl@U?$max_work_groups@$01@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$id@$01@12@XZ +??$get_info_impl@U?$max_work_groups@$02@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$id@$02@12@XZ +??$get_info_impl@U?$max_work_item_sizes@$00@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$range@$00@12@XZ +??$get_info_impl@U?$max_work_item_sizes@$01@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$range@$01@12@XZ +??$get_info_impl@U?$max_work_item_sizes@$02@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$range@$02@12@XZ +??$get_info_impl@Uaddress_bits@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uarchitecture@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBA?AW4architecture@experimental@oneapi@ext@12@XZ +??$get_info_impl@Uaspects@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4aspect@_V1@sycl@@V?$allocator@W4aspect@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Uatomic64@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uatomic_fence_order_capabilities@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4memory_order@_V1@sycl@@V?$allocator@W4memory_order@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Uatomic_fence_scope_capabilities@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4memory_scope@_V1@sycl@@V?$allocator@W4memory_scope@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Uatomic_memory_order_capabilities@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4memory_order@_V1@sycl@@V?$allocator@W4memory_order@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Uatomic_memory_scope_capabilities@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4memory_scope@_V1@sycl@@V?$allocator@W4memory_scope@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Uattributes@kernel@info@_V1@sycl@@@kernel@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Ubackend_version@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Ubuilt_in_kernel_ids@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@Vkernel_id@_V1@sycl@@V?$allocator@Vkernel_id@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Ubuilt_in_kernels@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@Vstring@detail@_V1@sycl@@V?$allocator@Vstring@detail@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Ucomponent_devices@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@Vdevice@_V1@sycl@@V?$allocator@Vdevice@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Ucomposite_device@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBA?AV012@XZ +??$get_info_impl@Ucontext@kernel@info@_V1@sycl@@@kernel@_V1@sycl@@AEBA?AVcontext@12@XZ +??$get_info_impl@Udevice_id@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Udevice_type@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AW4device_type@info@12@XZ +??$get_info_impl@Udouble_fp_config@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4fp_config@info@_V1@sycl@@V?$allocator@W4fp_config@info@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Udriver_version@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uerror_correction_support@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uexecution_capabilities@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4execution_capability@info@_V1@sycl@@V?$allocator@W4execution_capability@info@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Uext_intel_device_info_uuid@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$array@E$0BA@@std@@XZ +??$get_info_impl@Uext_intel_gpu_eu_count@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uext_intel_gpu_eu_count_per_subslice@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uext_intel_gpu_eu_simd_width@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uext_intel_gpu_hw_threads_per_eu@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uext_intel_gpu_slices@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uext_intel_gpu_subslices_per_slice@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uext_intel_max_mem_bandwidth@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uext_intel_mem_channel@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uext_intel_pci_address@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uext_oneapi_bfloat16_math_functions@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uext_oneapi_max_global_work_groups@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uext_oneapi_max_work_groups_1d@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$id@$00@12@XZ +??$get_info_impl@Uext_oneapi_max_work_groups_2d@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$id@$01@12@XZ +??$get_info_impl@Uext_oneapi_max_work_groups_3d@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$id@$02@12@XZ +??$get_info_impl@Uext_oneapi_srgb@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uextensions@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@Vstring@detail@_V1@sycl@@V?$allocator@Vstring@detail@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Uextensions@platform@info@_V1@sycl@@@platform@_V1@sycl@@AEBA?AV?$vector@Vstring@detail@_V1@sycl@@V?$allocator@Vstring@detail@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Ufree_memory@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Ufunction_name@kernel@info@_V1@sycl@@@kernel@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uglobal_mem_cache_line_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uglobal_mem_cache_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uglobal_mem_cache_type@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AW4global_mem_cache_type@info@12@XZ +??$get_info_impl@Uglobal_mem_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Ugpu_eu_count@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Ugpu_eu_count_per_subslice@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Ugpu_eu_simd_width@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Ugpu_hw_threads_per_eu@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Ugpu_slices@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Ugpu_subslices_per_slice@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uhalf_fp_config@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4fp_config@info@_V1@sycl@@V?$allocator@W4fp_config@info@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Uhost_unified_memory@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uimage2d_max_height@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uimage2d_max_width@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uimage3d_max_depth@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uimage3d_max_height@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uimage3d_max_width@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uimage_max_array_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uimage_max_buffer_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uimage_row_pitch_align@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uimage_support@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uis_available@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uis_compiler_available@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uis_endian_little@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uis_linker_available@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Ukernel_kernel_pipe_support@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Ulocal_mem_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Ulocal_mem_type@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AW4local_mem_type@info@12@XZ +??$get_info_impl@Umatrix_combinations@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@Ucombination@matrix@experimental@oneapi@ext@_V1@sycl@@V?$allocator@Ucombination@matrix@experimental@oneapi@ext@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Umax_clock_frequency@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_compute_queue_indices@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBAHXZ +??$get_info_impl@Umax_compute_units@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_constant_args@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_constant_buffer_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Umax_global_work_groups@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Umax_image_linear_height@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_image_linear_row_pitch@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_image_linear_width@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_mem_alloc_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Umax_mem_bandwidth@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Umax_num_sub_groups@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_parameter_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Umax_read_image_args@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_registers_per_work_group@device@info@experimental@codeplay@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_samplers@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_work_group_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Umax_work_item_dimensions@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umax_write_image_args@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umem_base_addr_align@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umemory_bus_width@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umemory_clock_rate@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Umipmap_max_anisotropy@device@info@experimental@oneapi@ext@_V1@sycl@@@device@_V1@sycl@@AEBAMXZ +??$get_info_impl@Uname@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uname@platform@info@_V1@sycl@@@platform@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Unative_vector_width_char@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Unative_vector_width_double@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Unative_vector_width_float@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Unative_vector_width_half@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Unative_vector_width_int@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Unative_vector_width_long@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Unative_vector_width_short@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Unum_args@kernel@info@_V1@sycl@@@kernel@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uopencl_c_version@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uparent_device@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV012@XZ +??$get_info_impl@Upartition_affinity_domains@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4partition_affinity_domain@info@_V1@sycl@@V?$allocator@W4partition_affinity_domain@info@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Upartition_max_sub_devices@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Upartition_properties@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4partition_property@info@_V1@sycl@@V?$allocator@W4partition_property@info@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Upartition_type_affinity_domain@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AW4partition_affinity_domain@info@12@XZ +??$get_info_impl@Upartition_type_property@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AW4partition_property@info@12@XZ +??$get_info_impl@Upci_address@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uplatform@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AVplatform@12@XZ +??$get_info_impl@Upreferred_interop_user_sync@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Upreferred_vector_width_char@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Upreferred_vector_width_double@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Upreferred_vector_width_float@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Upreferred_vector_width_half@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Upreferred_vector_width_int@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Upreferred_vector_width_long@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Upreferred_vector_width_short@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uprintf_buffer_size@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uprofile@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uprofile@platform@info@_V1@sycl@@@platform@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uprofiling_timer_resolution@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_KXZ +??$get_info_impl@Uqueue_profiling@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Ureference_count@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Ureference_count@kernel@info@_V1@sycl@@@kernel@_V1@sycl@@AEBAIXZ +??$get_info_impl@Usingle_fp_config@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@W4fp_config@info@_V1@sycl@@V?$allocator@W4fp_config@info@_V1@sycl@@@std@@@std@@XZ +??$get_info_impl@Usub_group_independent_forward_progress@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Usub_group_sizes@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$vector@_KV?$allocator@_K@std@@@std@@XZ +??$get_info_impl@Usupports_fusion@device@info@experimental@codeplay@ext@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uusm_device_allocations@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uusm_host_allocations@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uusm_restricted_shared_allocations@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uusm_shared_allocations@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uusm_system_allocations@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA_NXZ +??$get_info_impl@Uuuid@device@info@intel@ext@_V1@sycl@@@device@_V1@sycl@@AEBA?AV?$array@E$0BA@@std@@XZ +??$get_info_impl@Uvendor@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uvendor@platform@info@_V1@sycl@@@platform@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uvendor_id@device@info@_V1@sycl@@@device@_V1@sycl@@AEBAIXZ +??$get_info_impl@Uversion@device@info@_V1@sycl@@@device@_V1@sycl@@AEBA?AVstring@detail@12@XZ +??$get_info_impl@Uversion@platform@info@_V1@sycl@@@platform@_V1@sycl@@AEBA?AVstring@detail@12@XZ ??$get_profiling_info@Ucommand_end@event_profiling@info@_V1@sycl@@@event@_V1@sycl@@QEBA_KXZ ??$get_profiling_info@Ucommand_start@event_profiling@info@_V1@sycl@@@event@_V1@sycl@@QEBA_KXZ ??$get_profiling_info@Ucommand_submit@event_profiling@info@_V1@sycl@@@event@_V1@sycl@@QEBA_KXZ @@ -538,6 +538,7 @@ ??0exception@_V1@sycl@@IEAA@Verror_code@std@@AEBV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@4@HV?$shared_ptr@Vcontext@_V1@sycl@@@4@@Z ??0exception@_V1@sycl@@IEAA@Verror_code@std@@PEBDHV?$shared_ptr@Vcontext@_V1@sycl@@@4@@Z ??0exception@_V1@sycl@@IEAA@Verror_code@std@@V?$shared_ptr@Vcontext@_V1@sycl@@@4@AEBV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@4@@Z +??0exception@_V1@sycl@@IEAA@Verror_code@std@@V?$shared_ptr@Vcontext@_V1@sycl@@@4@PEBD@Z ??0exception@_V1@sycl@@QEAA@AEBV012@@Z ??0exception@_V1@sycl@@QEAA@HAEBVerror_category@std@@@Z ??0exception@_V1@sycl@@QEAA@HAEBVerror_category@std@@AEBV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@4@@Z @@ -1040,7 +1041,9 @@ ?end_recording@modifiable_command_graph@detail@experimental@oneapi@ext@_V1@sycl@@QEAA_NXZ ?ext_codeplay_supports_fusion@queue@_V1@sycl@@QEBA_NXZ ?ext_intel_read_host_pipe@handler@_V1@sycl@@AEAAXAEBV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@PEAX_K_N@Z +?ext_intel_read_host_pipe@handler@_V1@sycl@@AEAAXVstring_view@detail@23@PEAX_K_N@Z ?ext_intel_write_host_pipe@handler@_V1@sycl@@AEAAXAEBV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@PEAX_K_N@Z +?ext_intel_write_host_pipe@handler@_V1@sycl@@AEAAXVstring_view@detail@23@PEAX_K_N@Z ?ext_oneapi_advise_usm_cmd_buffer@MemoryManager@detail@_V1@sycl@@SAXV?$shared_ptr@Vcontext_impl@detail@_V1@sycl@@@std@@PEAU_pi_ext_command_buffer@@PEBX_KW4_pi_mem_advice@@V?$vector@IV?$allocator@I@std@@@6@PEAI@Z ?ext_oneapi_architecture_is@device@_V1@sycl@@QEAA_NW4arch_category@experimental@oneapi@ext@23@@Z ?ext_oneapi_architecture_is@device@_V1@sycl@@QEAA_NW4architecture@experimental@oneapi@ext@23@@Z @@ -1189,7 +1192,7 @@ ?getImageNumberChannels@detail@_V1@sycl@@YAEW4image_channel_order@23@@Z ?getImageType@image_impl@detail@_V1@sycl@@AEAA?AW4_pi_mem_type@@XZ ?getInteropContext@SYCLMemObjT@detail@_V1@sycl@@UEBA?AV?$shared_ptr@Vcontext_impl@detail@_V1@sycl@@@std@@XZ -?getKernelName@handler@_V1@sycl@@AEAA?AV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@XZ +?getKernelName@handler@_V1@sycl@@AEAA?AVstring@detail@23@XZ ?getMaxWorkGroups@handler@_V1@sycl@@AEAA?AV?$optional@V?$array@_K$02@std@@@std@@XZ ?getMaxWorkGroups_v2@handler@_V1@sycl@@AEAA?AV?$tuple@V?$array@_K$02@std@@_N@std@@XZ ?getMemoryObject@AccessorBaseHost@detail@_V1@sycl@@QEBAPEAXXZ @@ -1308,7 +1311,7 @@ ?get_kernel_bundle_impl@detail@_V1@sycl@@YA?AV?$shared_ptr@Vkernel_bundle_impl@detail@_V1@sycl@@@std@@AEBVcontext@23@AEBV?$vector@Vdevice@_V1@sycl@@V?$allocator@Vdevice@_V1@sycl@@@std@@@5@AEBV?$vector@Vkernel_id@_V1@sycl@@V?$allocator@Vkernel_id@_V1@sycl@@@std@@@5@W4bundle_state@23@@Z ?get_kernel_bundle_impl@detail@_V1@sycl@@YA?AV?$shared_ptr@Vkernel_bundle_impl@detail@_V1@sycl@@@std@@AEBVcontext@23@AEBV?$vector@Vdevice@_V1@sycl@@V?$allocator@Vdevice@_V1@sycl@@@std@@@5@W4bundle_state@23@@Z ?get_kernel_bundle_impl@detail@_V1@sycl@@YA?AV?$shared_ptr@Vkernel_bundle_impl@detail@_V1@sycl@@@std@@AEBVcontext@23@AEBV?$vector@Vdevice@_V1@sycl@@V?$allocator@Vdevice@_V1@sycl@@@std@@@5@W4bundle_state@23@AEBV?$function@$$A6A_NAEBV?$shared_ptr@Vdevice_image_impl@detail@_V1@sycl@@@std@@@Z@5@@Z -?get_kernel_id_impl@detail@_V1@sycl@@YA?AVkernel_id@23@V?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@@Z +?get_kernel_id_impl@detail@_V1@sycl@@YA?AVkernel_id@23@Vstring_view@123@@Z ?get_kernel_ids@_V1@sycl@@YA?AV?$vector@Vkernel_id@_V1@sycl@@V?$allocator@Vkernel_id@_V1@sycl@@@std@@@std@@XZ ?get_kernel_ids@kernel_bundle_plain@detail@_V1@sycl@@QEBA?AV?$vector@Vkernel_id@_V1@sycl@@V?$allocator@Vkernel_id@_V1@sycl@@@std@@@std@@XZ ?get_max_statement_size@stream@_V1@sycl@@QEBA_KXZ @@ -5171,6 +5174,7 @@ ?usesPinnedHostMemory@SYCLMemObjT@detail@_V1@sycl@@UEBA_NXZ ?verifyKernelInvoc@handler@_V1@sycl@@AEAAXAEBVkernel@23@@Z ?verifyUsedKernelBundle@handler@_V1@sycl@@AEAAXAEBV?$basic_string@DU?$char_traits@D@std@@V?$allocator@D@2@@std@@@Z +?verifyUsedKernelBundleInternal@handler@_V1@sycl@@AEAAXVstring_view@detail@23@@Z ?wait@event@_V1@sycl@@QEAAXXZ ?wait@event@_V1@sycl@@SAXAEBV?$vector@Vevent@_V1@sycl@@V?$allocator@Vevent@_V1@sycl@@@std@@@std@@@Z ?wait@queue@_V1@sycl@@QEAAXAEBUcode_location@detail@23@@Z diff --git a/sycl/test/abi/symbol_size_alignment.cpp b/sycl/test/abi/symbol_size_alignment.cpp index fc9308d1682ca..ba1c683d55ad5 100644 --- a/sycl/test/abi/symbol_size_alignment.cpp +++ b/sycl/test/abi/symbol_size_alignment.cpp @@ -52,9 +52,9 @@ int main() { check(); check(); #ifdef _MSC_VER - check(); + 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; }