[SYCL] Query pipe name from registration

The pipe name is generated in integration footer and will be available to the runtime during device image registration.

The runtime then store host pipe information in host piep map entry, which is kept track of in program manager.

The host pipe information can be queried from the program manager through getHostPipeEntry using the host pipe pointer that is determined by its class member __pipe.

Author: sherry-yuan

sycl/include/sycl/ext/intel/experimental/host_pipes.hpp

@@ -49,9 +49,19 @@ class
     host_pipe<_name, _dataT, _propertiesT,
               std::enable_if_t<sycl::ext::oneapi::experimental::
                                    is_property_list_v<_propertiesT>>> {
-  static_assert(
-      sycl::ext::oneapi::experimental::is_property_list_v<_propertiesT>,
-      "Host pipe is available only through new property list");
+
+  struct
+#ifdef __SYCL_DEVICE_ONLY__
+  [[__sycl_detail__::add_ir_global_variable_attributes(
+    "sycl-host-pipe",
+    nullptr
+    )]]
+  [[__sycl_detail__::host_pipe]]
+  [[__sycl_detail__::global_variable_allowed]] // may not be needed
+#endif
+  __pipeType { const char __p; };
+  
+  static constexpr __pipeType __pipe = {0};  
 
 public:
   using value_type = _dataT;

sycl/source/detail/host_pipe.cpp

@@ -7,6 +7,8 @@
 //===----------------------------------------------------------------------===//
 
 #include <sycl/ext/intel/experimental/host_pipes.hpp>
+#include <detail/host_pipe_map_entry.hpp>
+#include <detail/program_manager/program_manager.hpp>
 
 __SYCL_INLINE_NAMESPACE(cl) {
 namespace sycl {
@@ -27,7 +29,9 @@ host_pipe<_name, _dataT, _propertiesT,
   }
   // TODO: get pipe name from the pipe registration
   _dataT data;
-  const std::string pipe_name = "pipename";
+  const void* HostPipePtr = &__pipe;
+  detail::HostPipeMapEntry hostPipeEntry = detail::ProgramManager::getInstance().getHostPipeEntry(HostPipePtr);
+  const std::string pipe_name = hostPipeEntry.MUniqueId;
   size_t size = 4;
   event e = q.submit([=](handler &CGH) {
     CGH.read_write_host_pipe(pipe_name, (void *)(&data), (size_t)size, false,
@@ -50,7 +54,9 @@ void host_pipe<
     return;
   }
   // TODO: get pipe name from the pipe registration
-  const std::string pipe_name = "pipename";
+  const void* HostPipePtr = &__pipe;
+  detail::HostPipeMapEntry hostPipeEntry = detail::ProgramManager::getInstance().getHostPipeEntry(HostPipePtr);
+  const std::string pipe_name = hostPipeEntry.MUniqueId;
   const void *data_ptr = &data;
   size_t size = 4;
   event e = q.submit([=](handler &CGH) {