[SYCL][host_task] Align host_task event submission clock with start/end clock (#18377)

The submission time for host_task events was previously obtained using
`std::chrono::steady_clock`, while the command start and end times were
derived from `high_resolution_clock`. This discrepancy in clock epochs
led to meaningless duration calculations when users used submission time
as a reference.

This update standardizes the clock source by switching the submission
time to use `high_resolution_clock`, ensuring consistent and meaningful
timing results for host_task events.

Note: `steady_clock` is not related to wall clock. See
https://en.cppreference.com/w/cpp/chrono/steady_clock

Author: Nuullll

sycl/source/detail/event_impl.cpp

@@ -581,9 +581,9 @@ void event_impl::setSubmissionTime() {
   } else {
     // Returning host time
     using namespace std::chrono;
-    MSubmitTime =
-        duration_cast<nanoseconds>(steady_clock::now().time_since_epoch())
-            .count();
+    MSubmitTime = duration_cast<nanoseconds>(
+                      high_resolution_clock::now().time_since_epoch())
+                      .count();
   }
 }
 

sycl/test-e2e/Basic/profile_host_task.cpp

@@ -7,6 +7,8 @@
 #include <sycl/properties/all_properties.hpp>
 
 int main() {
+  const uint64_t timeout =
+      60ul * 1e9; // 60 second, large enough for executing an empty host_task
   sycl::queue q{{sycl::property::queue::enable_profiling()}};
 
   auto e = q.submit([&](sycl::handler &cgh) { cgh.host_task([=]() {}); });
@@ -29,10 +31,22 @@ int main() {
     return EXIT_FAILURE;
   }
 
+  if (start > submitted + timeout) {
+    std::cerr << "Invalid latency between command_submit and command_start: "
+              << (start - submitted) << " ns" << std::endl;
+    return EXIT_FAILURE;
+  }
+
   if (end < start) {
     std::cerr << "Invalid command_end time" << std::endl;
     return EXIT_FAILURE;
   }
 
+  if (end > start + timeout) {
+    std::cerr << "Invalid latency between command_start and command_end: "
+              << (end - start) << " ns" << std::endl;
+    return EXIT_FAILURE;
+  }
+
   return EXIT_SUCCESS;
 }