[SYCL][Graph] Add implementation and modify tests

Author: reble

sycl/include/sycl/ext/oneapi/experimental/enqueue_functions.hpp

@@ -12,6 +12,7 @@
 
 #include <sycl/detail/common.hpp>
 #include <sycl/event.hpp>
+#include <sycl/ext/oneapi/experimental/graph.hpp>
 #include <sycl/ext/oneapi/properties/properties.hpp>
 #include <sycl/handler.hpp>
 #include <sycl/nd_range.hpp>
@@ -103,13 +104,22 @@ void submit(queue Q, CommandGroupFunc &&CGF,
       Q, std::forward<CommandGroupFunc>(CGF), CodeLoc);
 }
 
+__SYCL_EXPORT void submit(queue Q, command_graph<graph_state::executable> G,
+                          const sycl::detail::code_location &CodeLoc =
+                              sycl::detail::code_location::current());
+
 template <typename CommandGroupFunc>
 event submit_with_event(queue Q, CommandGroupFunc &&CGF,
                         const sycl::detail::code_location &CodeLoc =
                             sycl::detail::code_location::current()) {
   return Q.submit(std::forward<CommandGroupFunc>(CGF), CodeLoc);
 }
 
+__SYCL_EXPORT event
+submit_with_event(queue Q, command_graph<graph_state::executable> G,
+                  const sycl::detail::code_location &CodeLoc =
+                      sycl::detail::code_location::current());
+
 template <typename KernelName = sycl::detail::auto_name, typename KernelType>
 void single_task(handler &CGH, const KernelType &KernelObj) {
   CGH.single_task<KernelName>(KernelObj);

sycl/source/enqueue_functions.cpp

@@ -38,6 +38,17 @@ __SYCL_EXPORT void mem_advise(queue Q, void *Ptr, size_t NumBytes, int Advice,
                            /*CallerNeedsEvent=*/false);
 }
 
+__SYCL_EXPORT event
+submit_with_event(queue Q, command_graph<graph_state::executable> G,
+                  const sycl::detail::code_location &CodeLoc) {
+  return Q.ext_oneapi_graph(G, CodeLoc);
+}
+
+__SYCL_EXPORT void submit(queue Q, command_graph<graph_state::executable> G,
+                          const sycl::detail::code_location &CodeLoc) {
+  Q.ext_oneapi_graph(G, CodeLoc);
+}
+
 } // namespace ext::oneapi::experimental
 } // namespace _V1
 } // namespace sycl

sycl/test-e2e/Graph/RecordReplay/ext_oneapi_enqueue_functions.cpp

@@ -43,7 +43,7 @@ int main() {
 
   auto GraphExec = Graph.finalize();
 
-  InOrderQueue.submit([&](handler &CGH) { CGH.ext_oneapi_graph(GraphExec); });
+  exp_ext::submit(InOrderQueue, GraphExec);
   InOrderQueue.wait_and_throw();
 
   free(PtrA, InOrderQueue);

sycl/test-e2e/Graph/RecordReplay/ext_oneapi_enqueue_functions_submit.cpp

@@ -60,7 +60,7 @@ int main() {
 
     auto GraphExec = Graph.finalize();
 
-    Queue.submit([&](handler &CGH) { CGH.ext_oneapi_graph(GraphExec); });
+    exp_ext::submit(Queue, GraphExec);
     Queue.wait_and_throw();
   }
 

sycl/test-e2e/Graph/RecordReplay/ext_oneapi_enqueue_functions_submit_with_event.cpp

@@ -52,8 +52,7 @@ int main() {
 
   auto GraphExec = Graph.finalize();
 
-  Queue.submit([&](handler &CGH) { CGH.ext_oneapi_graph(GraphExec); });
-  Queue.wait_and_throw();
+  exp_ext::submit_with_event(Queue, GraphExec).wait();
 
   free(PtrA, Queue);
   free(PtrB, Queue);