Make command_submit = command_start = command_end for NOP

Author: againull

sycl/source/detail/event_impl.cpp

@@ -348,7 +348,10 @@ event_impl::get_profiling_info<info::event_profiling::command_start>() {
       return get_event_profiling_info<info::event_profiling::command_start>(
           Handle, this->getAdapter());
     }
-    return 0;
+    // If command is nop (for example, USM operations for 0 bytes) return
+    // recorded submission time. If event is created using default constructor,
+    // 0 will be returned.
+    return MSubmitTime;
   }
   if (!MHostProfilingInfo)
     throw sycl::exception(
@@ -367,7 +370,10 @@ uint64_t event_impl::get_profiling_info<info::event_profiling::command_end>() {
       return get_event_profiling_info<info::event_profiling::command_end>(
           Handle, this->getAdapter());
     }
-    return 0;
+    // If command is nop (for example, USM operations for 0 bytes) return
+    // recorded submission time. If event is created using default constructor,
+    // 0 will be returned.
+    return MSubmitTime;
   }
   if (!MHostProfilingInfo)
     throw sycl::exception(

sycl/test-e2e/Regression/dummy_event_info.cpp

@@ -19,9 +19,13 @@ int main() {
   assert(e.get_info<info::event::command_execution_status>() ==
          info::event_command_status::complete);
   assert(e.get_info<info::event::reference_count>() == 0);
-  assert(e.get_profiling_info<sycl::info::event_profiling::command_submit>() ==
-         0);
-  assert(e.get_profiling_info<sycl::info::event_profiling::command_start>() ==
-         0);
-  assert(e.get_profiling_info<sycl::info::event_profiling::command_end>() == 0);
+  auto submit_time =
+      e.get_profiling_info<sycl::info::event_profiling::command_submit>();
+  auto start_time =
+      e.get_profiling_info<sycl::info::event_profiling::command_start>();
+  auto end_time =
+      e.get_profiling_info<sycl::info::event_profiling::command_end>();
+
+  assert(submit_time == start_time);
+  assert(start_time == end_time);
 }