[SYCL][UR][L0] Fix issue with event caching causing profiling tag conflicts

This commit adds a test and changes to a UR version that fixes an issue
where the L0 would report old timestamp recordings for events produced
for profiling tags, due to reusing of dead events.

Signed-off-by: Larsen, Steffen <[email protected]>

Author: steffenlarsen

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/steffenlarsen/unified-runtime")
   include(${CMAKE_CURRENT_SOURCE_DIR}/cmake/modules/UnifiedRuntimeTag.cmake)
 
   set(UMF_BUILD_EXAMPLES OFF CACHE INTERNAL "EXAMPLES")

sycl/cmake/modules/UnifiedRuntimeTag.cmake

@@ -1,7 +1 @@
-# commit eb076da108a49ef1426f38690547a71905f58015
-# Merge: d8d8ee90 46832dfd
-# Author: Callum Fare <[email protected]>
-# 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 b7b6b55769c2f4e8ffb077a9f945e371232148f2)

sycl/test-e2e/Regression/profiling_tag_cached_conflicting.cpp

@@ -0,0 +1,32 @@
+// REQUIRES: aspect-ext_oneapi_queue_profiling_tag
+// RUN: %{build} -o %t.out
+// RUN: %{run} %t.out
+
+// Regression test to ensure that the adapters do not tamper (e.g. through
+// caching the events) the recordings.
+
+// HIP backend currently returns invalid values for submission time queries.
+// UNSUPPORTED: hip
+// UNSUPPORTED-TRACKER: https://github.com/intel/llvm/issues/12904
+
+// CUDA backend seems to fail sporadically for expected profiling tag time
+// query orderings.
+// UNSUPPORTED: cuda
+// UNSUPPORTED-TRACKER: https://github.com/intel/llvm/issues/14053
+
+#include <sycl/sycl.hpp>
+
+int main() {
+  sycl::queue Q{sycl::property::queue::in_order()};
+
+  uint64_t T1 = 0;
+  for (size_t I = 0; I < 20; ++I) {
+    sycl::event E = sycl::ext::oneapi::experimental::submit_profiling_tag(Q);
+    uint64_t T2 =
+        E.get_profiling_info<sycl::info::event_profiling::command_end>();
+    assert(T1 < T2);
+    std::swap(T1, T2);
+  }
+
+  return 0;
+}