[SYCL][NFC] Modernize getting host accessor (#10224)

`get_access` for host accessor is deprecated by SYCL 2020 in favor of
`get_host_access`.

Note: this patch does not update all tests we have, there are still
major categories skipped like `XPTI`, `Sampler`, etc.

Author: AlexeySachkov

sycl/test-e2e/Basic/fpga_tests/buffer_location.cpp

@@ -17,7 +17,7 @@ int main() {
 
   Queue.wait();
 
-  auto Acc = Buf.template get_access<sycl::access::mode::read_write>();
+  auto Acc = Buf.get_host_access();
   assert(Acc[0] == 42 && "Value mismatch");
 
   return 0;

sycl/test-e2e/Basic/fpga_tests/fpga_io_pipes.cpp

@@ -77,7 +77,7 @@ int test_io_nb_pipe(sycl::queue Queue) {
     });
   });
 
-  auto readHostBuffer = writeBuf.get_access<sycl::access::mode::read>();
+  auto readHostBuffer = writeBuf.get_host_access();
   if (readHostBuffer[0] != InputData) {
     std::cout << "Read from a file mismatches " << readHostBuffer[0]
               << " Vs expected " << InputData << std::endl;
@@ -102,7 +102,7 @@ int test_io_bl_pipe(sycl::queue Queue) {
     });
   });
 
-  auto readHostBuffer = writeBuf.get_access<sycl::access::mode::read>();
+  auto readHostBuffer = writeBuf.get_host_access();
   if (readHostBuffer[0] != InputData) {
     std::cout << "Read from a file mismatches " << readHostBuffer[0]
               << " Vs expected " << InputData << std::endl;

sycl/test-e2e/Basic/fpga_tests/fpga_pipes_legacy_ns.cpp

@@ -41,7 +41,7 @@ template <typename PipeName> int test_simple_nb_pipe(sycl::queue Queue) {
     });
   });
 
-  auto readHostBuffer = writeBuf.get_access<sycl::access::mode::read>();
+  auto readHostBuffer = writeBuf.get_host_access();
   if (readHostBuffer[0] != 42) {
     std::cout << "Result mismatches " << readHostBuffer[0] << " Vs expected "
               << 42 << std::endl;

sycl/test-e2e/Basic/fpga_tests/fpga_queue.cpp

@@ -116,7 +116,7 @@ int main() {
       return -1;
     }
 
-    auto readBufferC = bufC.get_access<access::mode::read>();
+    auto readBufferC = bufC.get_host_access();
     for (size_t i = 0; i != dataSize; ++i) {
       if (readBufferC[i] != 2 * i) {
         std::cout << "Result mismatches " << readBufferC[i] << " Vs expected "

sycl/test-e2e/Basic/handler/interop_task.cpp

@@ -48,7 +48,7 @@ int main() {
   });
 
   {
-    auto DstAcc = DstBuf.template get_access<sycl::access::mode::read_write>();
+    auto DstAcc = DstBuf.get_host_access();
     const int Expected = 42;
     for (int I = 0; I < DstAcc.get_count(); ++I)
       if (DstAcc[I] != Expected) {
@@ -59,8 +59,7 @@ int main() {
   }
 
   {
-    auto DstAcc2 =
-        DstBuf2.template get_access<sycl::access::mode::read_write>();
+    auto DstAcc2 = DstBuf2.get_host_access();
     const int Expected = 42;
     for (int I = 0; I < DstAcc2.get_count(); ++I)
       if (DstAcc2[I] != Expected) {

sycl/test-e2e/Basic/multisource.cpp

@@ -68,7 +68,7 @@ int main() {
 
     calc_buf(q, a, b, c, r);
 
-    auto C = c.get_access<access::mode::read>();
+    auto C = c.get_host_access();
     for (size_t i = 0; i < N; i++) {
       if (C[i] != 1) {
         std::cout << "Wrong value " << C[i] << " for element " << i

sycl/test-e2e/HostInteropTask/host-task.cpp

@@ -59,7 +59,7 @@ void test2(queue &Q) {
   });
 
   {
-    auto Acc = Buffer2.get_access<mode::read>();
+    auto Acc = Buffer2.get_host_access();
 
     for (size_t Idx = 0; Idx < Acc.get_count(); ++Idx) {
       std::cout << "Second buffer [" << Idx << "] = " << Acc[Idx] << std::endl;

sycl/test-e2e/HostInteropTask/interop-task.cpp

@@ -19,7 +19,7 @@ template <typename T> class Init;
 
 template <typename BufferT, typename ValueT>
 void checkBufferValues(BufferT Buffer, ValueT Value) {
-  auto Acc = Buffer.template get_access<mode::read>();
+  auto Acc = Buffer.get_host_access();
   for (size_t Idx = 0; Idx < Acc.get_count(); ++Idx) {
     if (Acc[Idx] != Value) {
       std::cerr << "buffer[" << Idx << "] = " << Acc[Idx]

sycl/test-e2e/InorderQueue/in_order_buffs.cpp

@@ -51,7 +51,7 @@ int main() {
       cgh.parallel_for<class ordered_reader>(myRange, myKernel);
     });
 
-    auto readBufferB = bufB.get_access<access::mode::read>();
+    auto readBufferB = bufB.get_host_access();
     for (size_t i = 0; i != dataSize; ++i) {
       if (readBufferB[i] != i) {
         std::cout << "Result mismatches " << readBufferB[i] << " vs expected "

sycl/test-e2e/KernelParams/array-kernel-param-nested-run.cpp

@@ -81,7 +81,7 @@ bool test_accessor_array_in_struct(queue &myQueue) {
           output_accessor[index] = S.a[0][index] + S.a[1][index] + S.x + S.y;
         });
   });
-  const auto HostAccessor = out_buffer.get_access<sycl::access::mode::read>();
+  const auto HostAccessor = out_buffer.get_host_access();
 
   return verify_1D("Accessor array in struct", c_num_items, output, ref);
 }
@@ -109,7 +109,7 @@ bool test_templated_array_in_struct(queue &myQueue) {
           output_accessor[index] = sint.a[index] + sll.a[index];
         });
   });
-  const auto HostAccessor = out_buffer.get_access<sycl::access::mode::read>();
+  const auto HostAccessor = out_buffer.get_host_access();
 
   return verify_1D("Templated array in struct", c_num_items, output, ref);
 }