From b7f3070fe460f74807a05a00cbf3b83ee030c397 Mon Sep 17 00:00:00 2001 From: Andrei Elovikov Date: Tue, 22 Nov 2022 13:05:25 -0800 Subject: [PATCH 1/2] [SYCL][Level Zero][USM] Add a test for read-only shared alloc For https://github.com/intel/llvm/pull/7496. --- SYCL/USM/shared_read_only.cpp | 22 ++++++++++++++++++++++ 1 file changed, 22 insertions(+) create mode 100644 SYCL/USM/shared_read_only.cpp diff --git a/SYCL/USM/shared_read_only.cpp b/SYCL/USM/shared_read_only.cpp new file mode 100644 index 0000000000..b0511497ea --- /dev/null +++ b/SYCL/USM/shared_read_only.cpp @@ -0,0 +1,22 @@ +// REQUIRES: level_zero +// RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple %s -o %t.out +// RUN: env ZE_DEBUG=1 %GPU_RUN_PLACEHOLDER %t.out h 2> %t1.out; cat %t1.out %GPU_CHECK_PLACEHOLDER + +#include + +int main() { + sycl::queue q; + auto *p1 = sycl::malloc_shared( + 42, q, {sycl::ext::oneapi::property::usm::device_read_only()}); + auto *p2 = sycl::malloc_shared(42, q); + + // CHECK: zeMemAllocShared + // CHECK: {{zeCommandListAppendMemAdvise.*ZE_MEMORY_ADVICE_SET_READ_MOSTLY}} + // CHECK: {{zeCommandListAppendMemAdvise.*ZE_MEMORY_ADVICE_SET_PREFERRED_LOCATION*}} + // CHECK: zeMemAllocShared + // CHECK-NOT: MemAdvise + + free(p2, q); + free(p1, q); + return 0; +} From 75da0465d0618bafe816c88588c8540995a88eed Mon Sep 17 00:00:00 2001 From: Andrei Elovikov Date: Wed, 23 Nov 2022 14:02:57 -0800 Subject: [PATCH 2/2] Address CR comment --- SYCL/USM/shared_read_only.cpp | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/SYCL/USM/shared_read_only.cpp b/SYCL/USM/shared_read_only.cpp index b0511497ea..0a16f9d195 100644 --- a/SYCL/USM/shared_read_only.cpp +++ b/SYCL/USM/shared_read_only.cpp @@ -1,6 +1,6 @@ // REQUIRES: level_zero // RUN: %clangxx -fsycl -fsycl-targets=%sycl_triple %s -o %t.out -// RUN: env ZE_DEBUG=1 %GPU_RUN_PLACEHOLDER %t.out h 2> %t1.out; cat %t1.out %GPU_CHECK_PLACEHOLDER +// RUN: env ZE_DEBUG=1 %GPU_RUN_PLACEHOLDER %t.out 2> %t1.out; cat %t1.out %GPU_CHECK_PLACEHOLDER #include