Implement backend content extension

Author: lbushi25

sycl/include/sycl/kernel_bundle.hpp

@@ -37,6 +37,7 @@
 #include <utility>     // for move
 #include <variant>     // for hash
 #include <vector>      // for vector
+#include <span>        // for span
 
 namespace sycl {
 inline namespace _V1 {
@@ -117,6 +118,12 @@ class __SYCL_EXPORT device_image_plain {
 protected:
   detail::DeviceImageImplPtr impl;
 
+  backend get_backend() const;
+
+  const std::byte *get_BinaryStart() const;
+
+  const std::byte *get_BinaryEnd() const;
+
   template <class Obj>
   friend const decltype(Obj::impl) &
   detail::getSyclObjImpl(const Obj &SyclObject);
@@ -145,6 +152,26 @@ class device_image : public detail::device_image_plain,
     return device_image_plain::has_kernel(KernelID, Dev);
   }
 
+  backend ext_oneapi_get_backend() const noexcept {
+    return device_image_plain::get_backend();
+  }
+
+  template <sycl::bundle_state T = State,
+            typename = std::enable_if_t<T == bundle_state::executable>>
+  std::vector<std::byte> ext_oneapi_get_backend_content() const {
+    return std::vector(device_image_plain::get_BinaryStart(),
+                       device_image_plain::get_BinaryEnd());
+  }
+
+#ifdef __cpp_lib_span
+  template <sycl::bundle_state T = State,
+            typename = std::enable_if_t<T == bundle_state::executable>>
+  std::span<std::byte> ext_oneapi_get_content_backend_view() const {
+    return std::span(device_image_plain::get_BinaryStart(),
+                     device_image_plain::get_BinaryEnd());
+  }
+#endif
+
 private:
   device_image(detail::DeviceImageImplPtr Impl)
       : device_image_plain(std::move(Impl)) {}

sycl/source/kernel_bundle.cpp

@@ -45,6 +45,20 @@ ur_native_handle_t device_image_plain::getNative() const {
   return impl->getNative();
 }
 
+backend device_image_plain::get_backend() const {
+  return impl->get_context().get_backend();
+}
+
+const std::byte *device_image_plain::get_BinaryStart() const {
+  return reinterpret_cast<const std::byte *>(
+      impl->get_bin_image_ref()->getRawData().BinaryStart);
+}
+
+const std::byte *device_image_plain::get_BinaryEnd() const {
+  return reinterpret_cast<const std::byte *>(
+      impl->get_bin_image_ref()->getRawData().BinaryEnd);
+}
+
 ////////////////////////////
 ///// kernel_bundle_plain
 ///////////////////////////