Add Python bindings for SYCL IPC memory via dpctl

dpctl/CMakeLists.txt

@@ -206,3 +206,4 @@ target_link_libraries(DpctlCAPI INTERFACE ${_trgt}_headers)
 add_subdirectory(program)
 add_subdirectory(memory)
 add_subdirectory(utils)
+add_subdirectory(ipc)

dpctl/_backend.pxd

@@ -101,6 +101,7 @@ cdef extern from "syclinterface/dpctl_sycl_enum_types.h":
         _emulated                           "emulated",
         _is_component                       "is_component",
         _is_composite                       "is_composite",
+        _ext_oneapi_ipc_memory              "ext_oneapi_ipc_memory",
 
     ctypedef enum _partition_affinity_domain_type \
             "DPCTLPartitionAffinityDomainType":
@@ -606,3 +607,19 @@ cdef extern from "syclinterface/dpctl_sycl_extension_interface.h":
         DPCTLSyclRawKernelArgRef Ref)
 
     cdef bint DPCTLRawKernelArg_Available()
+
+cdef extern from "syclinterface/dpctl_sycl_ipc_memory_interface.h":
+    cdef int DPCTLIPCMem_GetHandle(
+        DPCTLSyclUSMRef Ptr,
+        DPCTLSyclContextRef CRef,
+        char **DataOut,
+        size_t *SizeOut)
+    cdef DPCTLSyclUSMRef DPCTLIPCMem_OpenHandle(
+        const char *HandleData,
+        size_t HandleDataSize,
+        DPCTLSyclContextRef CRef,
+        DPCTLSyclDeviceRef DRef)
+    cdef void DPCTLIPCMem_CloseHandle(
+        DPCTLSyclUSMRef MappedPtr,
+        DPCTLSyclContextRef CRef)
+    cdef void DPCTLIPCMem_FreeHandleData(char *Data)

dpctl/_sycl_device.pyx

@@ -885,6 +885,18 @@ cdef class SyclDevice(_SyclDevice):
         cdef _aspect_type AT = _aspect_type._is_composite
         return DPCTLDevice_HasAspect(self._device_ref, AT)
 
+    @property
+    def has_aspect_ext_oneapi_ipc_memory(self):
+        """ Returns ``True`` if this device supports inter-process
+        communication (IPC) memory handles, ``False`` otherwise.
+
+        Returns:
+            bool:
+                Indicates if device supports IPC memory.
+        """
+        cdef _aspect_type AT = _aspect_type._ext_oneapi_ipc_memory
+        return DPCTLDevice_HasAspect(self._device_ref, AT)
+
     @property
     def image_2d_max_width(self):
         """ Returns the maximum width of a 2D image or 1D image in pixels.

dpctl/ipc/CMakeLists.txt

@@ -0,0 +1,10 @@
+if(DPCTL_HAS_IPC_MEMORY)
+    set(_cy_file ${CMAKE_CURRENT_SOURCE_DIR}/_ipc_memory.pyx)
+    get_filename_component(_trgt ${_cy_file} NAME_WLE)
+    build_dpctl_ext(${_trgt} ${_cy_file} "dpctl/ipc" RELATIVE_PATH "..")
+    target_link_libraries(DpctlCAPI INTERFACE ${_trgt}_headers)
+endif()
+
+# Always install __init__.py (handles graceful fallback when IPC not supported)
+install(FILES ${CMAKE_CURRENT_SOURCE_DIR}/__init__.py
+    DESTINATION ${CMAKE_INSTALL_PREFIX}/dpctl/ipc)

dpctl/ipc/__init__.pxd

@@ -0,0 +1,18 @@
+#                      Data Parallel Control (dpctl)
+#
+# Copyright 2020-2026 Intel Corporation
+#
+# Licensed under the Apache License, Version 2.0 (the "License");
+# you may not use this file except in compliance with the License.
+# You may obtain a copy of the License at
+#
+#    http://www.apache.org/licenses/LICENSE-2.0
+#
+# Unless required by applicable law or agreed to in writing, software
+# distributed under the License is distributed on an "AS IS" BASIS,
+# WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
+# See the License for the specific language governing permissions and
+# limitations under the License.
+
+# distutils: language = c++
+# cython: language_level=3

dpctl/ipc/__init__.py

@@ -0,0 +1,82 @@
+#                      Data Parallel Control (dpctl)
+#
+# Copyright 2020-2026 Intel Corporation
+#
+# Licensed under the Apache License, Version 2.0 (the "License");
+# you may not use this file except in compliance with the License.
+# You may obtain a copy of the License at
+#
+#    http://www.apache.org/licenses/LICENSE-2.0
+#
+# Unless required by applicable law or agreed to in writing, software
+# distributed under the License is distributed on an "AS IS" BASIS,
+# WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
+# See the License for the specific language governing permissions and
+# limitations under the License.
+
+"""
+**Data Parallel Control IPC** provides Python objects for inter-process
+communication of SYCL USM memory.
+
+- :class:`IPCMemoryHandle` wraps ``sycl::ext::oneapi::experimental::ipc::memory``
+  to export/import USM device pointers across processes.
+
+Requires oneAPI DPC++ compiler >= 2026.1 (with SYCL IPC memory runtime support).
+"""
+
+_IPC_MEMORY_AVAILABLE = False
+_IPC_MEMORY_ERROR = ""
+
+try:
+    from ._ipc_memory import IPCMemoryHandle
+    _IPC_MEMORY_AVAILABLE = True
+except ImportError as _e:
+    _IPC_MEMORY_ERROR = (
+        "dpctl.ipc.IPCMemoryHandle is not available. "
+        "SYCL IPC memory support was not detected at build time. "
+        "This requires oneAPI DPC++ compiler >= 2026.0 with "
+        "sycl::ext::oneapi::experimental::ipc::memory runtime support. "
+        f"(Import error: {_e})"
+    )
+
+    class IPCMemoryHandle:
+        """Placeholder for unavailable IPC memory support."""
+
+        def __init__(self, *args, **kwargs):
+            raise RuntimeError(_IPC_MEMORY_ERROR)
+
+        @staticmethod
+        def open(*args, **kwargs):
+            raise RuntimeError(_IPC_MEMORY_ERROR)
+
+        @staticmethod
+        def close_mapping(*args, **kwargs):
+            raise RuntimeError(_IPC_MEMORY_ERROR)
+
+
+def is_ipc_memory_supported():
+    """Return True if IPC memory is supported by the current SYCL runtime.
+
+    Returns:
+        bool: True if IPCMemoryHandle can be used, False otherwise.
+    """
+    return _IPC_MEMORY_AVAILABLE
+
+
+def check_ipc_memory_support():
+    """Raise RuntimeError if IPC memory is not supported.
+
+    Use this for early failure at application startup.
+
+    Raises:
+        RuntimeError: if the SYCL IPC memory API is not available.
+    """
+    if not _IPC_MEMORY_AVAILABLE:
+        raise RuntimeError(_IPC_MEMORY_ERROR)
+
+
+__all__ = [
+    "IPCMemoryHandle",
+    "is_ipc_memory_supported",
+    "check_ipc_memory_support",
+]

dpctl/ipc/_ipc_memory.pxd

@@ -0,0 +1,32 @@
+#                      Data Parallel Control (dpctl)
+#
+# Copyright 2020-2026 Intel Corporation
+#
+# Licensed under the Apache License, Version 2.0 (the "License");
+# you may not use this file except in compliance with the License.
+# You may obtain a copy of the License at
+#
+#    http://www.apache.org/licenses/LICENSE-2.0
+#
+# Unless required by applicable law or agreed to in writing, software
+# distributed under the License is distributed on an "AS IS" BASIS,
+# WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
+# See the License for the specific language governing permissions and
+# limitations under the License.
+
+# distutils: language = c++
+# cython: language_level=3
+
+"""Declarations for the IPCMemoryHandle Cython extension type."""
+
+from .._backend cimport DPCTLSyclContextRef, DPCTLSyclDeviceRef, DPCTLSyclUSMRef
+from .._sycl_context cimport SyclContext
+from .._sycl_device cimport SyclDevice
+from .._sycl_queue cimport SyclQueue
+from ..memory._memory cimport _Memory, MemoryUSMDevice
+
+
+cdef class IPCMemoryHandle:
+    cdef bytes _handle_bytes
+    cdef SyclContext _ctx
+    cdef bint _closed