diff --git a/sycl/test-e2e/AOT/Inputs/aot.cpp b/sycl/test-e2e/AOT/Inputs/aot.cpp index 4d70401464f49..d67efea47cad5 100644 --- a/sycl/test-e2e/AOT/Inputs/aot.cpp +++ b/sycl/test-e2e/AOT/Inputs/aot.cpp @@ -11,8 +11,8 @@ #include #include -constexpr sycl::access::mode sycl_read = sycl::access::mode::read; -constexpr sycl::access::mode sycl_write = sycl::access::mode::write; +constexpr sycl::access_mode sycl_read = sycl::access_mode::read; +constexpr sycl::access_mode sycl_write = sycl::access_mode::write; template class SimpleVadd; diff --git a/sycl/test-e2e/AOT/Inputs/simple.cpp b/sycl/test-e2e/AOT/Inputs/simple.cpp index c9a6bacbb3583..9cef56b960f50 100644 --- a/sycl/test-e2e/AOT/Inputs/simple.cpp +++ b/sycl/test-e2e/AOT/Inputs/simple.cpp @@ -8,7 +8,7 @@ int main() { sycl::buffer buf(&data, sycl::range<1>(1)); q.submit([&](sycl::handler &h) { - auto acc = buf.get_access(h); + auto acc = buf.get_access(h); h.single_task([=]() { acc[0] = 42; }); }).wait(); } diff --git a/sycl/test-e2e/BFloat16/bfloat16_conversions.cpp b/sycl/test-e2e/BFloat16/bfloat16_conversions.cpp index 1dfac131aac87..f68dd3d55bc4e 100644 --- a/sycl/test-e2e/BFloat16/bfloat16_conversions.cpp +++ b/sycl/test-e2e/BFloat16/bfloat16_conversions.cpp @@ -85,7 +85,7 @@ int test_device_vector_conversions(queue Q) { std::cout << "float[4] -> bfloat16[4] conversion on device..." << std::flush; // Convert float array to bfloat16 array Q.submit([&](handler &CGH) { - accessor ERR(err_buf, CGH); + accessor ERR(err_buf, CGH); CGH.single_task([=]() { float FloatArray[4] = {1.0f, -1.0f, 0.0f, 2.0f}; bfloat16 BF16Array[4]; @@ -106,7 +106,7 @@ int test_device_vector_conversions(queue Q) { std::cout << "bfloat16[4] -> float[4] conversion on device..." << std::flush; // Convert bfloat16 array back to float array Q.submit([&](handler &CGH) { - accessor ERR(err_buf, CGH); + accessor ERR(err_buf, CGH); CGH.single_task([=]() { bfloat16 BF16Array[3] = {1.0f, 0.0f, -1.0f}; float FloatArray[3]; diff --git a/sycl/test-e2e/BFloat16/bfloat16_type.hpp b/sycl/test-e2e/BFloat16/bfloat16_type.hpp index 542aa6a453aba..fced19d748952 100644 --- a/sycl/test-e2e/BFloat16/bfloat16_type.hpp +++ b/sycl/test-e2e/BFloat16/bfloat16_type.hpp @@ -18,7 +18,7 @@ template void assert_close(const T &C, const float ref) { void verify_conv_implicit(queue &q, buffer &a, range<1> &r, const float ref) { q.submit([&](handler &cgh) { - auto A = a.get_access(cgh); + auto A = a.get_access(cgh); cgh.parallel_for(r, [=](id<1> index) { sycl::ext::oneapi::bfloat16 AVal{A[index]}; A[index] = AVal; @@ -31,7 +31,7 @@ void verify_conv_implicit(queue &q, buffer &a, range<1> &r, void verify_conv_explicit(queue &q, buffer &a, range<1> &r, const float ref) { q.submit([&](handler &cgh) { - auto A = a.get_access(cgh); + auto A = a.get_access(cgh); cgh.parallel_for(r, [=](id<1> index) { sycl::ext::oneapi::bfloat16 AVal = A[index]; A[index] = float(AVal); @@ -46,9 +46,9 @@ void verify_add(queue &q, buffer &a, buffer &b, range<1> &r, buffer c{r}; q.submit([&](handler &cgh) { - auto A = a.get_access(cgh); - auto B = b.get_access(cgh); - auto C = c.get_access(cgh); + auto A = a.get_access(cgh); + auto B = b.get_access(cgh); + auto C = c.get_access(cgh); cgh.parallel_for(r, [=](id<1> index) { sycl::ext::oneapi::bfloat16 AVal{A[index]}; sycl::ext::oneapi::bfloat16 BVal{B[index]}; @@ -65,9 +65,9 @@ void verify_sub(queue &q, buffer &a, buffer &b, range<1> &r, buffer c{r}; q.submit([&](handler &cgh) { - auto A = a.get_access(cgh); - auto B = b.get_access(cgh); - auto C = c.get_access(cgh); + auto A = a.get_access(cgh); + auto B = b.get_access(cgh); + auto C = c.get_access(cgh); cgh.parallel_for(r, [=](id<1> index) { sycl::ext::oneapi::bfloat16 AVal{A[index]}; sycl::ext::oneapi::bfloat16 BVal{B[index]}; @@ -83,8 +83,8 @@ void verify_minus(queue &q, buffer &a, range<1> &r, const float ref) { buffer c{r}; q.submit([&](handler &cgh) { - auto A = a.get_access(cgh); - auto C = c.get_access(cgh); + auto A = a.get_access(cgh); + auto C = c.get_access(cgh); cgh.parallel_for(r, [=](id<1> index) { sycl::ext::oneapi::bfloat16 AVal{A[index]}; sycl::ext::oneapi::bfloat16 CVal = -AVal; @@ -100,9 +100,9 @@ void verify_mul(queue &q, buffer &a, buffer &b, range<1> &r, buffer c{r}; q.submit([&](handler &cgh) { - auto A = a.get_access(cgh); - auto B = b.get_access(cgh); - auto C = c.get_access(cgh); + auto A = a.get_access(cgh); + auto B = b.get_access(cgh); + auto C = c.get_access(cgh); cgh.parallel_for(r, [=](id<1> index) { sycl::ext::oneapi::bfloat16 AVal{A[index]}; sycl::ext::oneapi::bfloat16 BVal{B[index]}; @@ -119,9 +119,9 @@ void verify_div(queue &q, buffer &a, buffer &b, range<1> &r, buffer c{r}; q.submit([&](handler &cgh) { - auto A = a.get_access(cgh); - auto B = b.get_access(cgh); - auto C = c.get_access(cgh); + auto A = a.get_access(cgh); + auto B = b.get_access(cgh); + auto C = c.get_access(cgh); cgh.parallel_for(r, [=](id<1> index) { sycl::ext::oneapi::bfloat16 AVal{A[index]}; sycl::ext::oneapi::bfloat16 BVal{B[index]}; @@ -138,9 +138,9 @@ void verify_logic(queue &q, buffer &a, buffer &b, buffer c{r}; q.submit([&](handler &cgh) { - auto A = a.get_access(cgh); - auto B = b.get_access(cgh); - auto C = c.get_access(cgh); + auto A = a.get_access(cgh); + auto B = b.get_access(cgh); + auto C = c.get_access(cgh); cgh.parallel_for(r, [=](id<1> index) { sycl::ext::oneapi::bfloat16 AVal{A[index]}; sycl::ext::oneapi::bfloat16 BVal{B[index]}; diff --git a/sycl/test-e2e/BFloat16/bfloat16_vec_builtins.cpp b/sycl/test-e2e/BFloat16/bfloat16_vec_builtins.cpp index 4955fb5234ce5..e2f8e55cf2ecc 100644 --- a/sycl/test-e2e/BFloat16/bfloat16_vec_builtins.cpp +++ b/sycl/test-e2e/BFloat16/bfloat16_vec_builtins.cpp @@ -81,8 +81,7 @@ bool check(bool a, bool b) { return (a != b); } { /* On Device */ \ buffer err_buf(&err, 1); \ q.submit([&](handler &cgh) { \ - accessor ERR(err_buf, \ - cgh); \ + accessor ERR(err_buf, cgh); \ cgh.single_task([=]() { OPTEST(NAME, SZ, RETTY, INPVAL) }); \ }).wait(); \ } \ @@ -131,7 +130,7 @@ void test() { { buffer err_buf(&err, 1); q.submit([&](handler &cgh) { - accessor ERR(err_buf, cgh); + accessor ERR(err_buf, cgh); cgh.single_task([=]() { vec arg{1.0f, nan, 2.0f}; vec res = sycl::ext::oneapi::experimental::isnan(arg); @@ -220,7 +219,7 @@ void test() { { buffer err_buf(&err, 1); q.submit([&](handler &cgh) { - accessor ERR(err_buf, cgh); + accessor ERR(err_buf, cgh); cgh.single_task([=]() { vec arg1, arg2, arg3; bfloat16 inpVal1 = 1.0f; diff --git a/sycl/test-e2e/DeviceCodeSplit/Inputs/split-per-source-second-file.cpp b/sycl/test-e2e/DeviceCodeSplit/Inputs/split-per-source-second-file.cpp index 67d5a1f752b24..64d15867ea483 100644 --- a/sycl/test-e2e/DeviceCodeSplit/Inputs/split-per-source-second-file.cpp +++ b/sycl/test-e2e/DeviceCodeSplit/Inputs/split-per-source-second-file.cpp @@ -15,7 +15,7 @@ void runKernelsFromFile2() { assert(KernelIDStorage[0] == KernelID1); Q.submit([&](sycl::handler &Cgh) { - auto Acc = Buf.get_access(Cgh); + auto Acc = Buf.get_access(Cgh); Cgh.single_task([=]() { Acc[0] = 3; }); }); } diff --git a/sycl/test-e2e/DeviceCodeSplit/grf.cpp b/sycl/test-e2e/DeviceCodeSplit/grf.cpp index b2b0cbfa09194..d7b4eece4553a 100644 --- a/sycl/test-e2e/DeviceCodeSplit/grf.cpp +++ b/sycl/test-e2e/DeviceCodeSplit/grf.cpp @@ -85,7 +85,7 @@ int main(void) { << "\n"; auto e = q.submit([&](handler &cgh) { - auto PA = bufa.get_access(cgh); + auto PA = bufa.get_access(cgh); cgh.parallel_for(Size, [=](id<1> i) { PA[i] += 2; }); }); @@ -116,7 +116,7 @@ int main(void) { << "\n"; auto e = q.submit([&](handler &cgh) { - auto PA = bufa.get_access(cgh); + auto PA = bufa.get_access(cgh); cgh.parallel_for(Size, KernelFunctor(PA, prop)); }); diff --git a/sycl/test-e2e/DeviceCodeSplit/grf_512.cpp b/sycl/test-e2e/DeviceCodeSplit/grf_512.cpp index 282fbd65196ed..69ff90711aeb8 100644 --- a/sycl/test-e2e/DeviceCodeSplit/grf_512.cpp +++ b/sycl/test-e2e/DeviceCodeSplit/grf_512.cpp @@ -63,7 +63,7 @@ int main(void) { << "\n"; auto e = q.submit([&](handler &cgh) { - auto PA = bufa.get_access(cgh); + auto PA = bufa.get_access(cgh); cgh.parallel_for(Size, [=](id<1> i) { PA[i] += 2; }); }); @@ -90,7 +90,7 @@ int main(void) { << "\n"; auto e = q.submit([&](handler &cgh) { - auto PA = bufa.get_access(cgh); + auto PA = bufa.get_access(cgh); cgh.parallel_for(Size, KernelFunctor(PA, prop)); }); diff --git a/sycl/test-e2e/DeviceCodeSplit/split-per-kernel.cpp b/sycl/test-e2e/DeviceCodeSplit/split-per-kernel.cpp index 7503ef6db464b..f6808ee7ccc6f 100644 --- a/sycl/test-e2e/DeviceCodeSplit/split-per-kernel.cpp +++ b/sycl/test-e2e/DeviceCodeSplit/split-per-kernel.cpp @@ -25,7 +25,7 @@ int main() { assert(!KB.has_kernel(KernelID3)); Q.submit([&](sycl::handler &Cgh) { - auto Acc = Buf.get_access(Cgh); + auto Acc = Buf.get_access(Cgh); Cgh.single_task([=]() { Acc[0] = 1; }); }); } @@ -44,7 +44,7 @@ int main() { assert(!KB.has_kernel(KernelID3)); Q.submit([&](sycl::handler &Cgh) { - auto Acc = Buf.get_access(Cgh); + auto Acc = Buf.get_access(Cgh); Cgh.single_task([=]() { Acc[0] = 2; }); }); } @@ -63,7 +63,7 @@ int main() { assert(!KB.has_kernel(KernelID2)); Q.submit([&](sycl::handler &Cgh) { - auto Acc = Buf.get_access(Cgh); + auto Acc = Buf.get_access(Cgh); Cgh.single_task([=]() { Acc[0] = 3; }); }); } diff --git a/sycl/test-e2e/DeviceCodeSplit/split-per-source-main.cpp b/sycl/test-e2e/DeviceCodeSplit/split-per-source-main.cpp index 6ebfd6226be52..ecdae516bb9a3 100644 --- a/sycl/test-e2e/DeviceCodeSplit/split-per-source-main.cpp +++ b/sycl/test-e2e/DeviceCodeSplit/split-per-source-main.cpp @@ -31,7 +31,7 @@ int main() { { sycl::buffer Buf(&Data, sycl::range<1>(1)); Q.submit([&](sycl::handler &Cgh) { - auto Acc = Buf.get_access(Cgh); + auto Acc = Buf.get_access(Cgh); Cgh.single_task([=]() { Acc[0] = 1; }); }); } @@ -40,7 +40,7 @@ int main() { { sycl::buffer Buf(&Data, sycl::range<1>(1)); Q.submit([&](sycl::handler &Cgh) { - auto Acc = Buf.get_access(Cgh); + auto Acc = Buf.get_access(Cgh); Cgh.single_task([=]() { Acc[0] = 2; }); }); } diff --git a/sycl/test-e2e/NewOffloadDriver/Inputs/aot.cpp b/sycl/test-e2e/NewOffloadDriver/Inputs/aot.cpp index 39aed079cd935..23004de46c6f3 100644 --- a/sycl/test-e2e/NewOffloadDriver/Inputs/aot.cpp +++ b/sycl/test-e2e/NewOffloadDriver/Inputs/aot.cpp @@ -11,8 +11,8 @@ #include #include -constexpr sycl::access::mode sycl_read = sycl::access::mode::read; -constexpr sycl::access::mode sycl_write = sycl::access::mode::write; +constexpr sycl::access_mode sycl_read = sycl::access_mode::read; +constexpr sycl::access_mode sycl_write = sycl::access_mode::write; template class Vadd; diff --git a/sycl/test-e2e/NewOffloadDriver/Inputs/split-per-source-second-file.cpp b/sycl/test-e2e/NewOffloadDriver/Inputs/split-per-source-second-file.cpp index 67d5a1f752b24..64d15867ea483 100644 --- a/sycl/test-e2e/NewOffloadDriver/Inputs/split-per-source-second-file.cpp +++ b/sycl/test-e2e/NewOffloadDriver/Inputs/split-per-source-second-file.cpp @@ -15,7 +15,7 @@ void runKernelsFromFile2() { assert(KernelIDStorage[0] == KernelID1); Q.submit([&](sycl::handler &Cgh) { - auto Acc = Buf.get_access(Cgh); + auto Acc = Buf.get_access(Cgh); Cgh.single_task([=]() { Acc[0] = 3; }); }); } diff --git a/sycl/test-e2e/NewOffloadDriver/multisource.cpp b/sycl/test-e2e/NewOffloadDriver/multisource.cpp index 69cdc8a53850b..d6fc22a847d4e 100644 --- a/sycl/test-e2e/NewOffloadDriver/multisource.cpp +++ b/sycl/test-e2e/NewOffloadDriver/multisource.cpp @@ -38,7 +38,7 @@ void init_buf(queue &q, buffer &b, range<1> &r, int i); #elif INIT_KERNEL void init_buf(queue &q, buffer &b, range<1> &r, int i) { q.submit([&](handler &cgh) { - auto B = b.get_access(cgh); + auto B = b.get_access(cgh); cgh.parallel_for(r, [=](id<1> index) { B[index] = i; }); }); } @@ -51,9 +51,9 @@ void calc_buf(queue &q, buffer &a, buffer &b, buffer &c, void calc_buf(queue &q, buffer &a, buffer &b, buffer &c, range<1> &r) { q.submit([&](handler &cgh) { - auto A = a.get_access(cgh); - auto B = b.get_access(cgh); - auto C = c.get_access(cgh); + auto A = a.get_access(cgh); + auto B = b.get_access(cgh); + auto C = c.get_access(cgh); cgh.parallel_for( r, [=](id<1> index) { C[index] = A[index] - B[index]; }); }); diff --git a/sycl/test-e2e/NewOffloadDriver/separate_compile.cpp b/sycl/test-e2e/NewOffloadDriver/separate_compile.cpp index 17dce9f7ee559..417b3251acfa7 100644 --- a/sycl/test-e2e/NewOffloadDriver/separate_compile.cpp +++ b/sycl/test-e2e/NewOffloadDriver/separate_compile.cpp @@ -37,7 +37,7 @@ int run_test_b(int v) { sycl::queue deviceQueue; sycl::buffer buf(arr, 1); deviceQueue.submit([&](sycl::handler &cgh) { - auto acc = buf.get_access(cgh); + auto acc = buf.get_access(cgh); cgh.single_task([=]() { acc[0] *= 3; }); }); } @@ -62,7 +62,7 @@ int run_test_a(int v) { sycl::queue deviceQueue; sycl::buffer buf(arr, 1); deviceQueue.submit([&](sycl::handler &cgh) { - auto acc = buf.get_access(cgh); + auto acc = buf.get_access(cgh); cgh.single_task([=]() { acc[0] *= 2; }); }); } diff --git a/sycl/test-e2e/NewOffloadDriver/split-per-source-main.cpp b/sycl/test-e2e/NewOffloadDriver/split-per-source-main.cpp index 2ace230f83316..0b67bfb1752c9 100644 --- a/sycl/test-e2e/NewOffloadDriver/split-per-source-main.cpp +++ b/sycl/test-e2e/NewOffloadDriver/split-per-source-main.cpp @@ -31,7 +31,7 @@ int main() { { sycl::buffer Buf(&Data, sycl::range<1>(1)); Q.submit([&](sycl::handler &Cgh) { - auto Acc = Buf.get_access(Cgh); + auto Acc = Buf.get_access(Cgh); Cgh.single_task([=]() { Acc[0] = 1; }); }); } @@ -40,7 +40,7 @@ int main() { { sycl::buffer Buf(&Data, sycl::range<1>(1)); Q.submit([&](sycl::handler &Cgh) { - auto Acc = Buf.get_access(Cgh); + auto Acc = Buf.get_access(Cgh); Cgh.single_task([=]() { Acc[0] = 2; }); }); } diff --git a/sycl/test-e2e/SeparateCompile/same-kernel.cpp b/sycl/test-e2e/SeparateCompile/same-kernel.cpp index 27b701a0b1550..4a78b556a7808 100644 --- a/sycl/test-e2e/SeparateCompile/same-kernel.cpp +++ b/sycl/test-e2e/SeparateCompile/same-kernel.cpp @@ -22,8 +22,8 @@ using namespace sycl; class TestFnObj { public: TestFnObj(buffer &buf, handler &cgh) - : data(buf.get_access(cgh)) {} - accessor data; + : data(buf.get_access(cgh)) {} + accessor data; void operator()(id<1> item) const { data[item] = item[0]; } }; diff --git a/sycl/test-e2e/SeparateCompile/sycl-external-within-staticlib.cpp b/sycl/test-e2e/SeparateCompile/sycl-external-within-staticlib.cpp index d62becf4d5567..30364dee717b7 100644 --- a/sycl/test-e2e/SeparateCompile/sycl-external-within-staticlib.cpp +++ b/sycl/test-e2e/SeparateCompile/sycl-external-within-staticlib.cpp @@ -36,9 +36,9 @@ void hostf(unsigned Size, sycl::buffer &bufA, sycl::buffer &bufB, sycl::buffer &bufC) { sycl::range<1> range{Size}; sycl::queue().submit([&](sycl::handler &cgh) { - auto accA = bufA.get_access(cgh); - auto accB = bufB.get_access(cgh); - auto accC = bufC.get_access(cgh); + auto accA = bufA.get_access(cgh); + auto accB = bufB.get_access(cgh); + auto accC = bufC.get_access(cgh); cgh.parallel_for(range, [=](sycl::id<1> ID) { accC[ID] = external_f1(accA[ID], accB[ID]); diff --git a/sycl/test-e2e/SeparateCompile/sycl-external.cpp b/sycl/test-e2e/SeparateCompile/sycl-external.cpp index 85e2c97d6512a..537b380a51d5a 100644 --- a/sycl/test-e2e/SeparateCompile/sycl-external.cpp +++ b/sycl/test-e2e/SeparateCompile/sycl-external.cpp @@ -41,9 +41,9 @@ int main(void) { sycl::buffer bufC(C, range); sycl::queue().submit([&](sycl::handler &cgh) { - auto accA = bufA.get_access(cgh); - auto accB = bufB.get_access(cgh); - auto accC = bufC.get_access(cgh); + auto accA = bufA.get_access(cgh); + auto accB = bufB.get_access(cgh); + auto accC = bufC.get_access(cgh); cgh.parallel_for( range, [=](sycl::id<1> ID) { accC[ID] = foo(accA[ID], accB[ID]); }); diff --git a/sycl/test-e2e/SeparateCompile/test.cpp b/sycl/test-e2e/SeparateCompile/test.cpp index aee9f949da0f5..8a02b1b7d3996 100644 --- a/sycl/test-e2e/SeparateCompile/test.cpp +++ b/sycl/test-e2e/SeparateCompile/test.cpp @@ -74,7 +74,7 @@ int run_test_b(int v) { sycl::queue deviceQueue; sycl::buffer buf(arr, 1); deviceQueue.submit([&](sycl::handler &cgh) { - auto acc = buf.get_access(cgh); + auto acc = buf.get_access(cgh); cgh.single_task([=]() { acc[0] *= 3; }); }); } @@ -99,7 +99,7 @@ int run_test_a(int v) { sycl::queue deviceQueue; sycl::buffer buf(arr, 1); deviceQueue.submit([&](sycl::handler &cgh) { - auto acc = buf.get_access(cgh); + auto acc = buf.get_access(cgh); cgh.single_task([=]() { acc[0] *= 2; }); }); }