Undisbale graph extensions

Author: ianayl

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

@@ -8,13 +8,26 @@
 
 #pragma once
 
+#include <string>
+
 namespace sycl {
 inline namespace _V1 {
 namespace ext::oneapi::experimental {
 
 /// @brief Indicates the destination device for USM data to be prefetched to.
 enum class prefetch_type { device, host };
 
+inline std::string prefetchTypeToString(prefetch_type value) {
+  switch (value) {
+  case sycl::ext::oneapi::experimental::prefetch_type::device:
+    return "prefetch_type::device";
+  case sycl::ext::oneapi::experimental::prefetch_type::host:
+    return "prefetch_type::host";
+  default:
+    return "prefetch_type::unknown";
+  }
+}
+
 } // namespace ext::oneapi::experimental
 } // namespace _V1
 } // namespace sycl

sycl/source/detail/graph_impl.hpp

@@ -245,16 +245,10 @@ class node_impl : public std::enable_shared_from_this<node_impl> {
       return createCGCopy<sycl::detail::CGPrefetchUSM>();
 #ifdef __INTEL_PREVIEW_BREAKING_CHANGES
     case sycl::detail::CGType::PrefetchUSMExp:
-      throw sycl::exception(sycl::make_error_code(errc::feature_not_supported),
-                            "Prefetch as a part of the experimental enqueue "
-                            "function extension is currently not supported by "
-                            "SYCL Graph extension.");
-      // return createCGCopy<sycl::detail::CGPrefetchUSMExp>();
+      return createCGCopy<sycl::detail::CGPrefetchUSMExp>();
 #else
     case sycl::detail::CGType::PrefetchUSMExpD2H:
-      throw sycl::exception(sycl::make_error_code(errc::feature_not_supported),
-                            "Prefetch from device to host is currently not "
-                            "supported by SYCL Graph extension.");
+      return createCGCopy<sycl::detail::CGPrefetchUSMExpD2H>();
 #endif
     case sycl::detail::CGType::AdviseUSM:
       return createCGCopy<sycl::detail::CGAdviseUSM>();
@@ -649,6 +643,31 @@ class node_impl : public std::enable_shared_from_this<node_impl> {
                << " Length: " << Prefetch->getLength() << "\\n";
       }
       break;
+#ifdef __INTEL_PREVIEW_BREAKING_CHANGES
+    case sycl::detail::CGType::PrefetchUSMExp:
+      Stream << "CGPrefetchUSMExp \\n";
+      if (Verbose) {
+        sycl::detail::CGPrefetchUSMExp *Prefetch =
+            static_cast<sycl::detail::CGPrefetchUSMExp *>(MCommandGroup.get());
+        Stream << "Dst: " << Prefetch->getDst()
+               << " Length: " << Prefetch->getLength() << " Type: "
+               << sycl::ext::oneapi::experimental::prefetchTypeToString(
+                      Prefetch->getPrefetchType())
+               << "\\n";
+      }
+      break;
+#else
+    case sycl::detail::CGType::PrefetchUSMExpD2H:
+      Stream << "CGPrefetchUSM (Experimental, Device-To-Host) \\n";
+      if (Verbose) {
+        sycl::detail::CGPrefetchUSMExpD2H *Prefetch =
+            static_cast<sycl::detail::CGPrefetchUSMExpD2H *>(
+                MCommandGroup.get());
+        Stream << "Dst: " << Prefetch->getDst()
+               << " Length: " << Prefetch->getLength() << "\\n";
+      }
+      break;
+#endif
     case sycl::detail::CGType::AdviseUSM:
       Stream << "CGAdviseUSM \\n";
       if (Verbose) {