Removed aspect_host, select_host_device, has_host_device

Host device has been removed from DPC++ compiler in 2023.0.0

Also removed support for host device type and for backend host.

Author: oleksandr-pavlyk

dpctl/__init__.py

@@ -48,12 +48,10 @@
     has_accelerator_devices,
     has_cpu_devices,
     has_gpu_devices,
-    has_host_device,
     select_accelerator_device,
     select_cpu_device,
     select_default_device,
     select_gpu_device,
-    select_host_device,
 )
 from ._sycl_event import SyclEvent
 from ._sycl_platform import SyclPlatform, get_platforms, lsplatform

dpctl/_backend.pxd

@@ -37,7 +37,6 @@ cdef extern from "syclinterface/dpctl_sycl_enum_types.h":
     ctypedef enum _backend_type 'DPCTLSyclBackendType':
         _ALL_BACKENDS    'DPCTL_ALL_BACKENDS'
         _CUDA            'DPCTL_CUDA'
-        _HOST            'DPCTL_HOST'
         _LEVEL_ZERO      'DPCTL_LEVEL_ZERO'
         _OPENCL          'DPCTL_OPENCL'
         _UNKNOWN_BACKEND 'DPCTL_UNKNOWN_BACKEND'
@@ -49,7 +48,6 @@ cdef extern from "syclinterface/dpctl_sycl_enum_types.h":
         _CPU            'DPCTL_CPU'
         _CUSTOM         'DPCTL_CUSTOM'
         _GPU            'DPCTL_GPU'
-        _HOST_DEVICE    'DPCTL_HOST_DEVICE'
         _UNKNOWN_DEVICE 'DPCTL_UNKNOWN_DEVICE'
 
     ctypedef enum _arg_data_type 'DPCTLKernelArgType':
@@ -236,7 +234,6 @@ cdef extern from "syclinterface/dpctl_sycl_device_selector_interface.h":
     DPCTLSyclDeviceSelectorRef DPCTLCPUSelector_Create()
     DPCTLSyclDeviceSelectorRef DPCTLFilterSelector_Create(const char *)
     DPCTLSyclDeviceSelectorRef DPCTLGPUSelector_Create()
-    DPCTLSyclDeviceSelectorRef DPCTLHostSelector_Create()
     void DPCTLDeviceSelector_Delete(DPCTLSyclDeviceSelectorRef)
     int DPCTLDeviceSelector_Score(DPCTLSyclDeviceSelectorRef, DPCTLSyclDeviceRef)
 

dpctl/_sycl_device.pyx

@@ -162,8 +162,6 @@ cdef list _get_devices(DPCTLDeviceVectorRef DVRef):
 cdef str _backend_type_to_filter_string_part(_backend_type BTy):
     if BTy == _backend_type._CUDA:
         return "cuda"
-    elif BTy == _backend_type._HOST:
-        return "host"
     elif BTy == _backend_type._LEVEL_ZERO:
         return "level_zero"
     elif BTy == _backend_type._OPENCL:
@@ -181,8 +179,6 @@ cdef str _device_type_to_filter_string_part(_device_type DTy):
         return "cpu"
     elif DTy == _device_type._GPU:
         return "gpu"
-    elif DTy == _device_type._HOST_DEVICE:
-        return "host"
     else:
         return "unknown"
 
@@ -222,7 +218,6 @@ cdef class SyclDevice(_SyclDevice):
           :func:`dpctl.select_cpu_device()`,
           :func:`dpctl.select_default_device()`,
           :func:`dpctl.select_gpu_device()`,
-          :func:`dpctl.select_host_device()`.
 
 
         :Example:
@@ -359,8 +354,6 @@ cdef class SyclDevice(_SyclDevice):
         )
         if BTy == _backend_type._CUDA:
             return backend_type.cuda
-        elif BTy == _backend_type._HOST:
-            return backend_type.host
         elif BTy == _backend_type._LEVEL_ZERO:
             return backend_type.level_zero
         elif BTy == _backend_type._OPENCL:
@@ -388,21 +381,9 @@ cdef class SyclDevice(_SyclDevice):
             return device_type.cpu
         elif DTy == _device_type._GPU:
             return device_type.gpu
-        elif DTy == _device_type._HOST_DEVICE:
-            return device_type.host
         else:
             raise ValueError("Unknown device type.")
 
-    @property
-    def has_aspect_host(self):
-        """ Returns True if this device is a host device, False otherwise.
-
-        Returns:
-            bool: Indicates if the device is a host device.
-        """
-        cdef _aspect_type AT = _aspect_type._host
-        return DPCTLDevice_HasAspect(self._device_ref, AT)
-
     @property
     def has_aspect_cpu(self):
         """ Returns True if this device is a CPU device, False otherwise.

dpctl/_sycl_device_factory.pxd

@@ -31,10 +31,8 @@ cpdef SyclDevice select_accelerator_device()
 cpdef SyclDevice select_cpu_device()
 cpdef SyclDevice select_default_device()
 cpdef SyclDevice select_gpu_device()
-cpdef SyclDevice select_host_device()
 cpdef list get_devices(backend=*, device_type=*)
 cpdef int get_num_devices(backend=*, device_type=*)
 cpdef cpp_bool has_gpu_devices()
 cpdef cpp_bool has_cpu_devices()
 cpdef cpp_bool has_accelerator_devices()
-cpdef cpp_bool has_host_device()

dpctl/_sycl_device_factory.pyx

@@ -39,7 +39,6 @@ from ._backend cimport (  # noqa: E211
     DPCTLDeviceVector_Size,
     DPCTLDeviceVectorRef,
     DPCTLGPUSelector_Create,
-    DPCTLHostSelector_Create,
     DPCTLSyclDeviceRef,
     DPCTLSyclDeviceSelectorRef,
     _backend_type,
@@ -56,12 +55,10 @@ __all__ = [
     "select_cpu_device",
     "select_default_device",
     "select_gpu_device",
-    "select_host_device",
     "get_num_devices",
     "has_cpu_devices",
     "has_gpu_devices",
     "has_accelerator_devices",
-    "has_host_device",
 ]
 
 
@@ -71,8 +68,6 @@ cdef _backend_type _string_to_dpctl_sycl_backend_ty(str backend_str):
         return _backend_type._ALL_BACKENDS
     elif backend_str == "cuda":
         return _backend_type._CUDA
-    elif backend_str == "host":
-        return _backend_type._HOST
     elif backend_str == "level_zero":
         return _backend_type._LEVEL_ZERO
     elif backend_str == "opencl":
@@ -95,8 +90,6 @@ cdef _device_type _string_to_dpctl_sycl_device_ty(str dty_str):
         return _device_type._CUSTOM
     elif dty_str == "gpu":
         return _device_type._GPU
-    elif dty_str == "host":
-        return _device_type._HOST_DEVICE
     else:
         return _device_type._UNKNOWN_DEVICE
 
@@ -106,8 +99,6 @@ cdef _backend_type _enum_to_dpctl_sycl_backend_ty(BTy):
         return _backend_type._ALL_BACKENDS
     elif BTy == backend_type.cuda:
         return _backend_type._CUDA
-    elif BTy == backend_type.host:
-        return _backend_type._HOST
     elif BTy == backend_type.level_zero:
         return _backend_type._LEVEL_ZERO
     elif BTy == backend_type.opencl:
@@ -129,8 +120,6 @@ cdef _device_type _enum_to_dpctl_sycl_device_ty(DTy):
         return _device_type._CUSTOM
     elif DTy == device_type_t.gpu:
         return _device_type._GPU
-    elif DTy == device_type_t.host:
-        return _device_type._HOST_DEVICE
     else:
         return _device_type._UNKNOWN_DEVICE
 
@@ -288,19 +277,6 @@ cpdef cpp_bool has_accelerator_devices():
     return <cpp_bool>num_accelerator_dev
 
 
-cpdef cpp_bool has_host_device():
-    """ A helper function to check if there are any SYCL Host devices available.
-
-    Returns:
-        bool: ``True`` if ``sycl::device_type::host`` devices are present,
-        ``False`` otherwise.
-    """
-    cdef int num_host_dev = DPCTLDeviceMgr_GetNumDevices(
-        _device_type._HOST_DEVICE
-    )
-    return <cpp_bool>num_host_dev
-
-
 cpdef SyclDevice select_accelerator_device():
     """ A wrapper for SYCL's ``accelerator_selector`` class.
 
@@ -379,23 +355,3 @@ cpdef SyclDevice select_gpu_device():
         raise SyclDeviceCreationError("Device unavailable.")
     Device = SyclDevice._create(DRef)
     return Device
-
-
-cpdef SyclDevice select_host_device():
-    """ A wrapper for SYCL's ``host_selector`` class.
-
-    Returns:
-        dpctl.SyclDevice: A Python object wrapping the SYCL ``device``
-        returned by the SYCL ``host_selector``.
-    Raises:
-        dpctl.SyclDeviceCreationError: If the SYCL ``host_selector`` is
-        unable to select a ``device``.
-    """
-    cdef DPCTLSyclDeviceSelectorRef DSRef = DPCTLHostSelector_Create()
-    cdef DPCTLSyclDeviceRef DRef = DPCTLDevice_CreateFromSelector(DSRef)
-    # Free up the device selector
-    DPCTLDeviceSelector_Delete(DSRef)
-    if DRef is NULL:
-        raise SyclDeviceCreationError("Host device is unavailable.")
-    Device = SyclDevice._create(DRef)
-    return Device

dpctl/_sycl_event.pyx

@@ -302,8 +302,6 @@ cdef class SyclEvent(_SyclEvent):
             return backend_type.opencl
         elif BE == _backend_type._LEVEL_ZERO:
             return backend_type.level_zero
-        elif BE == _backend_type._HOST:
-            return backend_type.host
         elif BE == _backend_type._CUDA:
             return backend_type.cuda
         else:

dpctl/_sycl_platform.pyx

@@ -251,8 +251,6 @@ cdef class SyclPlatform(_SyclPlatform):
         )
         if BTy == _backend_type._CUDA:
             return backend_type.cuda
-        elif BTy == _backend_type._HOST:
-            return backend_type.host
         elif BTy == _backend_type._LEVEL_ZERO:
             return backend_type.level_zero
         elif BTy == _backend_type._OPENCL:

dpctl/_sycl_queue.pyx

@@ -676,8 +676,6 @@ cdef class SyclQueue(_SyclQueue):
             return backend_type.opencl
         elif BE == _backend_type._LEVEL_ZERO:
             return backend_type.level_zero
-        elif BE == _backend_type._HOST:
-            return backend_type.host
         elif BE == _backend_type._CUDA:
             return backend_type.cuda
         else:

dpctl/enum_types.py

@@ -54,7 +54,6 @@ class device_type(Enum):
     cpu = auto()
     custom = auto()
     gpu = auto()
-    host = auto()
 
 
 class backend_type(Enum):
@@ -74,7 +73,6 @@ class backend_type(Enum):
 
     all = auto()
     cuda = auto()
-    host = auto()
     level_zero = auto()
     opencl = auto()
 

dpctl/tests/_device_attributes_checks.py

@@ -23,7 +23,6 @@
     dpctl.select_cpu_device,
     dpctl.select_default_device,
     dpctl.select_gpu_device,
-    dpctl.select_host_device,
 ]
 
 list_of_valid_filter_selectors = [
@@ -120,13 +119,6 @@ def check_sub_group_sizes(device):
     assert all(el > 0 for el in sg_sizes)
 
 
-def check_has_aspect_host(device):
-    try:
-        device.has_aspect_host
-    except Exception:
-        pytest.fail("has_aspect_host call failed")
-
-
 def check_has_aspect_cpu(device):
     try:
         device.has_aspect_cpu
@@ -634,7 +626,6 @@ def check_global_mem_cache_line_size(device):
     check_preferred_vector_width_float,
     check_preferred_vector_width_double,
     check_preferred_vector_width_half,
-    check_has_aspect_host,
     check_has_aspect_cpu,
     check_has_aspect_gpu,
     check_has_aspect_accelerator,

dpctl/tests/test_sycl_device_factory.py

@@ -27,24 +27,20 @@
     (bty.level_zero, dty.gpu),
     (bty.opencl, dty.gpu),
     (bty.opencl, dty.cpu),
-    (bty.host, dty.host),
 ]
 
 argument_list_2 = [
-    ("host", "host"),
     ("level_zero", "gpu"),
     ("opencl", "gpu"),
     ("opencl", "cpu"),
 ]
 
 list_of_backend_str = [
-    "host",
     "level_zero",
     "opencl",
 ]
 
 list_of_device_type_str = [
-    "host",
     "gpu",
     "cpu",
 ]