diff --git a/sycl/source/detail/buffer_impl.cpp b/sycl/source/detail/buffer_impl.cpp index 676f49a63007..48389490e956 100644 --- a/sycl/source/detail/buffer_impl.cpp +++ b/sycl/source/detail/buffer_impl.cpp @@ -52,12 +52,12 @@ void buffer_impl::addInteropObject( if (std::find(Handles.begin(), Handles.end(), ur::cast(MInteropMemObject)) == Handles.end()) { - const AdapterPtr &Adapter = getAdapter(); - Adapter->call( + adapter_impl &Adapter = getAdapter(); + Adapter.call( ur::cast(MInteropMemObject)); ur_native_handle_t NativeHandle = 0; - Adapter->call(MInteropMemObject, nullptr, - &NativeHandle); + Adapter.call(MInteropMemObject, nullptr, + &NativeHandle); Handles.push_back(NativeHandle); } } diff --git a/sycl/source/detail/sycl_mem_obj_t.cpp b/sycl/source/detail/sycl_mem_obj_t.cpp index 87fc643459b1..11b00538b14a 100644 --- a/sycl/source/detail/sycl_mem_obj_t.cpp +++ b/sycl/source/detail/sycl_mem_obj_t.cpp @@ -36,21 +36,20 @@ SYCLMemObjT::SYCLMemObjT(ur_native_handle_t MemObject, MSharedPtrStorage(nullptr), MHostPtrProvided(true), MOwnNativeHandle(OwnNativeHandle) { ur_context_handle_t Context = nullptr; - const AdapterPtr &Adapter = getAdapter(); + adapter_impl &Adapter = getAdapter(); ur_mem_native_properties_t MemProperties = { UR_STRUCTURE_TYPE_MEM_NATIVE_PROPERTIES, nullptr, OwnNativeHandle}; - Adapter->call( + Adapter.call( MemObject, MInteropContext->getHandleRef(), &MemProperties, &MInteropMemObject); // Get the size of the buffer in bytes - Adapter->call(MInteropMemObject, UR_MEM_INFO_SIZE, - sizeof(size_t), &MSizeInBytes, - nullptr); + Adapter.call(MInteropMemObject, UR_MEM_INFO_SIZE, + sizeof(size_t), &MSizeInBytes, nullptr); - Adapter->call(MInteropMemObject, UR_MEM_INFO_CONTEXT, - sizeof(Context), &Context, nullptr); + Adapter.call(MInteropMemObject, UR_MEM_INFO_CONTEXT, + sizeof(Context), &Context, nullptr); if (MInteropContext->getHandleRef() != Context) throw sycl::exception( @@ -84,7 +83,7 @@ SYCLMemObjT::SYCLMemObjT(ur_native_handle_t MemObject, MSharedPtrStorage(nullptr), MHostPtrProvided(true), MOwnNativeHandle(OwnNativeHandle) { ur_context_handle_t Context = nullptr; - const AdapterPtr &Adapter = getAdapter(); + adapter_impl &Adapter = getAdapter(); ur_image_desc_t Desc = {}; Desc.stype = UR_STRUCTURE_TYPE_IMAGE_DESC; @@ -101,12 +100,12 @@ SYCLMemObjT::SYCLMemObjT(ur_native_handle_t MemObject, ur_mem_native_properties_t NativeProperties = { UR_STRUCTURE_TYPE_MEM_NATIVE_PROPERTIES, nullptr, OwnNativeHandle}; - Adapter->call( + Adapter.call( MemObject, MInteropContext->getHandleRef(), &Format, &Desc, &NativeProperties, &MInteropMemObject); - Adapter->call(MInteropMemObject, UR_MEM_INFO_CONTEXT, - sizeof(Context), &Context, nullptr); + Adapter.call(MInteropMemObject, UR_MEM_INFO_CONTEXT, + sizeof(Context), &Context, nullptr); if (MInteropContext->getHandleRef() != Context) throw sycl::exception( @@ -157,14 +156,13 @@ void SYCLMemObjT::updateHostMemory() { releaseHostMem(MShadowCopy); if (MOpenCLInterop) { - const AdapterPtr &Adapter = getAdapter(); - Adapter->call(MInteropMemObject); + getAdapter().call(MInteropMemObject); } } -const AdapterPtr &SYCLMemObjT::getAdapter() const { +adapter_impl &SYCLMemObjT::getAdapter() const { assert((MInteropContext != nullptr) && "Trying to get Adapter from SYCLMemObjT with nullptr ContextImpl."); - return (MInteropContext->getAdapter()); + return *(MInteropContext->getAdapter()); } bool SYCLMemObjT::isInterop() const { return MOpenCLInterop; } diff --git a/sycl/source/detail/sycl_mem_obj_t.hpp b/sycl/source/detail/sycl_mem_obj_t.hpp index a0b5c6b24f52..e5f8b7a4d3bd 100644 --- a/sycl/source/detail/sycl_mem_obj_t.hpp +++ b/sycl/source/detail/sycl_mem_obj_t.hpp @@ -90,7 +90,7 @@ class SYCLMemObjT : public SYCLMemObjI { virtual ~SYCLMemObjT() = default; - const AdapterPtr &getAdapter() const; + adapter_impl &getAdapter() const; size_t getSizeInBytes() const noexcept override { return MSizeInBytes; } __SYCL2020_DEPRECATED("get_count() is deprecated, please use size() instead")