diff --git a/sycl/include/sycl/queue.hpp b/sycl/include/sycl/queue.hpp index 6b9494fbc865a..a458f92bdfe37 100644 --- a/sycl/include/sycl/queue.hpp +++ b/sycl/include/sycl/queue.hpp @@ -2886,10 +2886,6 @@ class __SYCL_EXPORT queue : public detail::OwnerLessBase { Rest...); } -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES - buffer &getAssertHappenedBuffer(); -#endif - event memcpyToDeviceGlobal(void *DeviceGlobalPtr, const void *Src, bool IsDeviceImageScope, size_t NumBytes, size_t Offset, diff --git a/sycl/source/detail/queue_impl.hpp b/sycl/source/detail/queue_impl.hpp index 890891644bbac..af8b6e5808bcd 100644 --- a/sycl/source/detail/queue_impl.hpp +++ b/sycl/source/detail/queue_impl.hpp @@ -107,9 +107,6 @@ class queue_impl { const async_handler &AsyncHandler, const property_list &PropList) : MDevice(Device), MContext(Context), MAsyncHandler(AsyncHandler), MPropList(PropList), MHostQueue(MDevice->is_host()), -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES - MAssertHappenedBuffer(range<1>{1}), -#endif MIsInorder(has_property()), MDiscardEvents( has_property()), @@ -291,9 +288,6 @@ class queue_impl { queue_impl(sycl::detail::pi::PiQueue PiQueue, const ContextImplPtr &Context, const async_handler &AsyncHandler) : MContext(Context), MAsyncHandler(AsyncHandler), MHostQueue(false), -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES - MAssertHappenedBuffer(range<1>{1}), -#endif MIsInorder(has_property()), MDiscardEvents( has_property()), @@ -316,9 +310,6 @@ class queue_impl { const async_handler &AsyncHandler, const property_list &PropList) : MContext(Context), MAsyncHandler(AsyncHandler), MPropList(PropList), MHostQueue(false), -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES - MAssertHappenedBuffer(range<1>{1}), -#endif MIsInorder(has_property()), MDiscardEvents( has_property()), @@ -688,12 +679,6 @@ class queue_impl { /// \return a native handle. pi_native_handle getNative(int32_t &NativeHandleDesc) const; -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES - buffer &getAssertHappenedBuffer() { - return MAssertHappenedBuffer; - } -#endif - void registerStreamServiceEvent(const EventImplPtr &Event) { std::lock_guard Lock(MStreamsServiceEventsMutex); MStreamsServiceEvents.push_back(Event); @@ -934,11 +919,6 @@ class queue_impl { /// need to emulate it with multiple native in-order queues. bool MEmulateOOO = false; -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES - // Buffer to store assert failure descriptor - buffer MAssertHappenedBuffer; -#endif - // This event is employed for enhanced dependency tracking with in-order queue // Access to the event should be guarded with MMutex EventImplPtr MLastEventPtr; diff --git a/sycl/source/queue.cpp b/sycl/source/queue.cpp index acaecf2696629..2c54ba42ab210 100644 --- a/sycl/source/queue.cpp +++ b/sycl/source/queue.cpp @@ -314,12 +314,6 @@ pi_native_handle queue::getNative(int32_t &NativeHandleDesc) const { return impl->getNative(NativeHandleDesc); } -#ifndef __INTEL_PREVIEW_BREAKING_CHANGES -buffer &queue::getAssertHappenedBuffer() { - return impl->getAssertHappenedBuffer(); -} -#endif - event queue::memcpyToDeviceGlobal(void *DeviceGlobalPtr, const void *Src, bool IsDeviceImageScope, size_t NumBytes, size_t Offset, diff --git a/sycl/test/abi/sycl_symbols_linux.dump b/sycl/test/abi/sycl_symbols_linux.dump index 06956ee8ec445..034e8f4423d8f 100644 --- a/sycl/test/abi/sycl_symbols_linux.dump +++ b/sycl/test/abi/sycl_symbols_linux.dump @@ -3793,7 +3793,6 @@ _ZN4sycl3_V15queue18throw_asynchronousEv _ZN4sycl3_V15queue20memcpyToDeviceGlobalEPvPKvbmmRKSt6vectorINS0_5eventESaIS6_EE _ZN4sycl3_V15queue20wait_and_throw_proxyERKNS0_6detail13code_locationE _ZN4sycl3_V15queue22memcpyFromDeviceGlobalEPvPKvbmmRKSt6vectorINS0_5eventESaIS6_EE -_ZN4sycl3_V15queue23getAssertHappenedBufferEv _ZN4sycl3_V15queue25ext_oneapi_submit_barrierERKNS0_6detail13code_locationE _ZN4sycl3_V15queue25ext_oneapi_submit_barrierERKSt6vectorINS0_5eventESaIS3_EERKNS0_6detail13code_locationE _ZN4sycl3_V15queue27submit_impl_and_postprocessESt8functionIFvRNS0_7handlerEEERKNS0_6detail13code_locationERKS2_IFvbbRNS0_5eventEEE diff --git a/sycl/test/abi/sycl_symbols_windows.dump b/sycl/test/abi/sycl_symbols_windows.dump index 105fb6d287021..3b414022e9358 100644 --- a/sycl/test/abi/sycl_symbols_windows.dump +++ b/sycl/test/abi/sycl_symbols_windows.dump @@ -1141,7 +1141,6 @@ ?getAccData@UnsampledImageAccessorBaseHost@detail@_V1@sycl@@QEAAAEAUAccHostDataT@234@XZ ?getAccessRange@AccessorBaseHost@detail@_V1@sycl@@QEAAAEAV?$range@$02@34@XZ ?getAccessRange@AccessorBaseHost@detail@_V1@sycl@@QEBAAEBV?$range@$02@34@XZ -?getAssertHappenedBuffer@queue@_V1@sycl@@AEAAAEAV?$buffer@UAssertHappened@detail@_V1@sycl@@$00V?$aligned_allocator@UAssertHappened@detail@_V1@sycl@@@234@X@23@XZ ?getBorderColor@detail@_V1@sycl@@YA?AV?$vec@M$03@23@W4image_channel_order@23@@Z ?getBufSizeForContext@SYCLMemObjT@detail@_V1@sycl@@SA_KAEBV?$shared_ptr@Vcontext_impl@detail@_V1@sycl@@@std@@_K@Z ?getChannelOrder@SampledImageAccessorBaseHost@detail@_V1@sycl@@QEBA?AW4image_channel_order@34@XZ