Finish off rewriting regression tests

sycl/test-e2e/Regression/pf-wg-atomic64.cpp

@@ -10,11 +10,12 @@ using AtomicRefT =
 
 int main() {
  queue q;
- auto *p = malloc_shared<unsigned long long>(1, q);
+ sycl::buffer<unsigned long long> p_buf{sycl::range{1}};
  try {
  q.submit([&](sycl::handler &cgh) {
+ sycl::accessor p{p_buf, cgh};
  cgh.parallel_for_work_group(range{1}, range{1}, [=](group<1>) {
- AtomicRefT feature(*p);
+ AtomicRefT feature(p[0]);
  feature += 42;
  });
  }).wait();

sycl/test-e2e/Regression/range-rounding-this-id.cpp

@@ -30,13 +30,17 @@ template <int D> void test(queue &q) {
  id<D> this_id;
  id<D> ref_id;
  };
- std::vector<T, usm_allocator<T, usm::alloc::shared>> vec(range.size(), q);
- auto *p = vec.data();
- q.parallel_for(range, [=](auto it) {
- p[it.get_linear_id()] = {sycl::ext::oneapi::experimental::this_id<D>(),
- it.get_id()};
- }).wait_and_throw();
-
+ std::vector<T> vec(range.size());
+ {
+ sycl::buffer<T> p_buf{vec};
+ q.submit([&](sycl::handler &h) {
+ sycl::accessor p{p_buf, h};
+ q.parallel_for(range, [=](auto it) {
+ p[it.get_linear_id()] = {sycl::ext::oneapi::experimental::this_id<D>(),
+ it.get_id()};
+ });
+ }).wait_and_throw();
+ } // p_buf goes out of scope here and writed back to vec
  for (const auto &[this_item, ref_item] : vec) {
  if (this_item != ref_item) {
  std::cout << "fail: " << this_item << " != " << ref_item << "\n";

sycl/test-e2e/Regression/reduction_64bit_atomic64.cpp

@@ -2,7 +2,7 @@
 // RUN: %{build} -o %t.out
 //
 // RUN: %{run} %t.out
-
+// REQUIRES: aspect-usm_shared_allocations
 // Tests that a previously known case for reduction doesn't cause a requirement
 // for atomic64.
 // TODO: When aspect requirements are added to testing, this test could be set