// REQUIRES: level_zero || cuda

// RUN: %{build} -o %t2.out
// RUN: env SYCL_UR_TRACE=2 UR_L0_DEBUG=1 %{run} %t2.out %if level_zero %{ 2>&1 | FileCheck %s %}
// RUN: %{run} %t2.out

#include <sycl/detail/core.hpp>

#include <cassert>
#include <string>

using namespace sycl;

int main() {
  {
    int data1[10] = {-1, -1, -1, -1, -1, -1, -1, -1, -1, -1};
    {
      buffer<int, 1> a(data1, range<1>(10), {property::buffer::use_host_ptr()});
      buffer<int, 1> b(
          range<1>(10),
          {ext::oneapi::property::buffer::use_pinned_host_memory()});
      queue myQueue;
      myQueue.submit([&](handler &cgh) {
        auto A = a.get_access<access::mode::read_write>(cgh);
        auto B = b.get_access<access::mode::read_write>(cgh);
        cgh.parallel_for<class init_b>(range<1>{10}, [=](id<1> index) {
          B[index] = 0;
          A[index] = B[index] + 1;
        });
      });
    } // Data is copied back because there is a user side shared_ptr
    for (int i = 0; i < 10; i++)
      assert(data1[i] == 1);
  }
}

// CHECK: <--- urMemBufferCreate
// CHECK: <--- urMemBufferCreate
// CHECK-SAME: UR_MEM_FLAG_ALLOC_HOST_POINTER