From 14cc9e778760be81f01541bf9387894a97d0ec14 Mon Sep 17 00:00:00 2001 From: "Zhao, Yang2" Date: Thu, 5 Dec 2024 09:31:22 +0100 Subject: [PATCH 1/2] add test --- .../common/options-statistics.cpp | 15 +++++++++++---- 1 file changed, 11 insertions(+), 4 deletions(-) diff --git a/sycl/test-e2e/AddressSanitizer/common/options-statistics.cpp b/sycl/test-e2e/AddressSanitizer/common/options-statistics.cpp index a36c5bbf1a5be..50ef733fc1d47 100644 --- a/sycl/test-e2e/AddressSanitizer/common/options-statistics.cpp +++ b/sycl/test-e2e/AddressSanitizer/common/options-statistics.cpp @@ -1,7 +1,8 @@ // REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O2 -g -o %t // RUN: %{run} %t 2>&1 | FileCheck %s -// RUN: env UR_LAYER_ASAN_OPTIONS=print_stats:1 %{run} %t 2>&1 | FileCheck --check-prefixes CHECK-STATS %s +// RUN: env UR_LAYER_ASAN_OPTIONS="print_stats:1;quarantine_size_mb:1" %{run} %t 2>&1 | FileCheck --check-prefixes CHECK-STATS %s +// RUN: env UR_LAYER_ASAN_OPTIONS="print_stats:1;quarantine_size_mb:0" %{run} %t 2>&1 | FileCheck --check-prefixes CHECK-STATS %s #include /// This test is used to check enabling/disabling memory overhead statistics @@ -12,20 +13,26 @@ constexpr std::size_t group_size = 1; int main() { sycl::queue Q; - int *array = sycl::malloc_device(1024 * 1024, Q); + int *array1 = sycl::malloc_device(10 * 1024 * 1024, Q); + int *array2 = sycl::malloc_device(10 * 1024 * 1024, Q); + int *array3 = sycl::malloc_device(10 * 1024 * 1024, Q); + + sycl::free(array2, Q); + sycl::free(array3, Q); Q.submit([&](sycl::handler &cgh) { auto acc = sycl::local_accessor(group_size, cgh); cgh.parallel_for( sycl::nd_range<1>(N, group_size), [=](sycl::nd_item<1> item) { - array[item.get_global_id()] = acc[item.get_local_id()]; + array1[item.get_global_id()] = acc[item.get_local_id()]; }); }); Q.wait(); // CHECK-STATS: Stats // CHECK-NOT: Stats - sycl::free(array, Q); + sycl::free(array1, Q); + std::cout << "PASS" << std::endl; return 0; } From 1928bf6145fba10c061c56f46dbd060e018963d8 Mon Sep 17 00:00:00 2001 From: "Zhao, Yang2" Date: Thu, 5 Dec 2024 09:40:02 +0100 Subject: [PATCH 2/2] update UR tag --- sycl/cmake/modules/FetchUnifiedRuntime.cmake | 2 +- sycl/cmake/modules/UnifiedRuntimeTag.cmake | 2 +- 2 files changed, 2 insertions(+), 2 deletions(-) diff --git a/sycl/cmake/modules/FetchUnifiedRuntime.cmake b/sycl/cmake/modules/FetchUnifiedRuntime.cmake index e9d52c5b23dac..d6a0251d63c86 100644 --- a/sycl/cmake/modules/FetchUnifiedRuntime.cmake +++ b/sycl/cmake/modules/FetchUnifiedRuntime.cmake @@ -116,7 +116,7 @@ if(SYCL_UR_USE_FETCH_CONTENT) CACHE PATH "Path to external '${name}' adapter source dir" FORCE) endfunction() - set(UNIFIED_RUNTIME_REPO "https://github.com/oneapi-src/unified-runtime") + set(UNIFIED_RUNTIME_REPO "https://github.com/zhaomaosu/unified-runtime.git") include(${CMAKE_CURRENT_SOURCE_DIR}/cmake/modules/UnifiedRuntimeTag.cmake) set(UMF_BUILD_EXAMPLES OFF CACHE INTERNAL "EXAMPLES") diff --git a/sycl/cmake/modules/UnifiedRuntimeTag.cmake b/sycl/cmake/modules/UnifiedRuntimeTag.cmake index bd50587d7a105..95db3fa23fdb6 100644 --- a/sycl/cmake/modules/UnifiedRuntimeTag.cmake +++ b/sycl/cmake/modules/UnifiedRuntimeTag.cmake @@ -4,4 +4,4 @@ # Date: Fri Nov 29 15:54:31 2024 +0000 # Merge pull request #2396 from kswiecicki/init-results-fix # [L0] Add nullopt check before init results access -set(UNIFIED_RUNTIME_TAG eb076da108a49ef1426f38690547a71905f58015) +set(UNIFIED_RUNTIME_TAG do-alloc-use-pool)