[SYCL] Implement buffer::get_access with range and offset

Signed-off-by: Mariya Podchishchaeva <[email protected]>

Author: Fznamznon

sycl/include/CL/sycl/accessor.hpp

@@ -763,7 +763,7 @@ class accessor
 #ifdef __SYCL_DEVICE_ONLY__
       ; // This ctor can't be used in device code, so no need to define it.
 #else   // !__SYCL_DEVICE_ONLY__
-      : __impl(detail::getSyclObjImpl(bufferRef)->BufPtr, Range,
+      : __impl((dataT *)detail::getSyclObjImpl(bufferRef)->BufPtr, Range,
                bufferRef.get_range(), Offset) {
     auto BufImpl = detail::getSyclObjImpl(bufferRef);
     if (AccessTarget == access::target::host_buffer) {

sycl/include/CL/sycl/buffer.hpp

@@ -153,20 +153,22 @@ class buffer {
     return impl->template get_access<T, dimensions, mode>(*this);
   }
 
-  // template <access::mode mode, access::target target =
-  // access::target::global_buffer> accessor<T, dimensions, mode, target,
-  // access::placeholder::false_t> get_access( handler &commandGroupHandler,
-  // range<dimensions> accessRange, id<dimensions> accessOffset = {}) {
-  //     return impl->get_access(commandGroupHandler, accessRange,
-  //     accessOffset);
-  // }
+  template <access::mode mode,
+            access::target target = access::target::global_buffer>
+  accessor<T, dimensions, mode, target, access::placeholder::false_t>
+  get_access(handler &commandGroupHandler, range<dimensions> accessRange,
+             id<dimensions> accessOffset = {}) {
+    return impl->template get_access<T, dimensions, mode, target>(
+        *this, commandGroupHandler, accessRange, accessOffset);
+  }
 
-  // template <access::mode mode>
-  // accessor<T, dimensions, mode, access::target::host_buffer,
-  // access::placeholder::false_t> get_access( range<dimensions> accessRange,
-  // id<dimensions> accessOffset = {}) {
-  //     return impl->get_access(accessRange, accessOffset);
-  // }
+  template <access::mode mode>
+  accessor<T, dimensions, mode, access::target::host_buffer,
+           access::placeholder::false_t>
+  get_access(range<dimensions> accessRange, id<dimensions> accessOffset = {}) {
+    return impl->template get_access<T, dimensions, mode>(*this, accessRange,
+                                                          accessOffset);
+  }
 
   template <typename Destination = std::nullptr_t>
   void set_final_data(Destination finalData = nullptr) {

sycl/include/CL/sycl/detail/buffer_impl.hpp

@@ -206,6 +206,26 @@ template <typename AllocatorT> class buffer_impl {
                     access::placeholder::false_t>(Buffer);
   }
 
+  template <typename T, int dimensions, access::mode mode,
+            access::target target = access::target::global_buffer>
+  accessor<T, dimensions, mode, target, access::placeholder::false_t>
+  get_access(buffer<T, dimensions, AllocatorT> &Buffer,
+             handler &commandGroupHandler, range<dimensions> accessRange,
+             id<dimensions> accessOffset) {
+    return accessor<T, dimensions, mode, target, access::placeholder::false_t>(
+        Buffer, commandGroupHandler, accessRange, accessOffset);
+  }
+
+  template <typename T, int dimensions, access::mode mode>
+  accessor<T, dimensions, mode, access::target::host_buffer,
+           access::placeholder::false_t>
+  get_access(buffer<T, dimensions, AllocatorT> &Buffer,
+             range<dimensions> accessRange, id<dimensions> accessOffset) {
+    return accessor<T, dimensions, mode, access::target::host_buffer,
+                    access::placeholder::false_t>(Buffer, accessRange,
+                                                  accessOffset);
+  }
+
 public:
   void moveMemoryTo(QueueImplPtr Queue, std::vector<cl::sycl::event> DepEvents,
                     EventImplPtr Event);