Merge pull request #1302 from IntelPython/update-for-cython-3

Update for cython 3

Author: oleksandr-pavlyk

.github/workflows/generate-coverage.yaml

@@ -79,7 +79,7 @@ jobs:
       - name: Install dpctl dependencies
         shell: bash -l {0}
         run: |
-          pip install numpy cython"<3" setuptools pytest pytest-cov scikit-build cmake coverage[toml]
+          pip install numpy cython setuptools pytest pytest-cov scikit-build cmake coverage[toml]
 
       - name: Build dpctl with coverage
         shell: bash -l {0}

.github/workflows/generate-docs.yml

@@ -49,7 +49,7 @@ jobs:
         if: ${{ !github.event.pull_request || github.event.action != 'closed' }}
         shell: bash -l {0}
         run: |
-          pip install numpy cython"<3" setuptools scikit-build cmake sphinx sphinx_rtd_theme pydot graphviz sphinxcontrib-programoutput sphinxcontrib-googleanalytics
+          pip install numpy cython setuptools scikit-build cmake sphinx sphinx_rtd_theme pydot graphviz sphinxcontrib-programoutput sphinxcontrib-googleanalytics
       - name: Checkout repo
         uses: actions/checkout@v3
         with:

.github/workflows/os-llvm-sycl-build.yml

@@ -108,7 +108,7 @@ jobs:
       - name: Install dpctl dependencies
         shell: bash -l {0}
         run: |
-          pip install numpy cython"<3" setuptools pytest scikit-build cmake
+          pip install numpy cython setuptools pytest scikit-build cmake
 
       - name: Checkout repo
         uses: actions/checkout@v3

conda-recipe/meta.yaml

@@ -20,7 +20,7 @@ requirements:
         - cmake  >=3.21
         - ninja
         - git
-        - cython  <3
+        - cython
         - python
         - scikit-build
         - numpy

dpctl/_backend.pxd

@@ -95,7 +95,6 @@ cdef extern from "syclinterface/dpctl_sycl_enum_types.h":
         _usm_device_allocations             'usm_device_allocations',
         _usm_host_allocations               'usm_host_allocations',
         _usm_shared_allocations             'usm_shared_allocations',
-        _usm_restricted_shared_allocations  'usm_restricted_shared_allocations',
         _usm_system_allocations             'usm_system_allocations',
         _usm_atomic_host_allocations        'usm_atomic_host_allocations',
         _usm_atomic_shared_allocations      'usm_atomic_shared_allocations',

dpctl/_sycl_context.pyx

@@ -68,7 +68,7 @@ cdef class SyclContextCreationError(Exception):
     pass
 
 
-cdef void _context_capsule_deleter(object o):
+cdef void _context_capsule_deleter(object o) noexcept:
     cdef DPCTLSyclContextRef CRef = NULL
     if pycapsule.PyCapsule_IsValid(o, "SyclContextRef"):
         CRef = <DPCTLSyclContextRef> pycapsule.PyCapsule_GetPointer(

dpctl/_sycl_device.pyx

@@ -597,20 +597,6 @@ cdef class SyclDevice(_SyclDevice):
         cdef _aspect_type AT = _aspect_type._usm_shared_allocations
         return DPCTLDevice_HasAspect(self._device_ref, AT)
 
-    @property
-    def has_aspect_usm_restricted_shared_allocations(self):
-        """ Returns True if this device supports USM memory
-        allocated as restricted USM, False otherwise.
-
-        Returns:
-            bool: Indicates that the device supports USM memory allocated using
-            ``sycl::malloc_shared`` as restricted USM.
-
-        .. deprecated:: 0.14
-        """
-        cdef _aspect_type AT = _aspect_type._usm_restricted_shared_allocations
-        return DPCTLDevice_HasAspect(self._device_ref, AT)
-
     @property
     def has_aspect_usm_system_allocations(self):
         """ Returns True if system allocator may be used instead of SYCL USM

dpctl/_sycl_event.pyx

@@ -73,7 +73,7 @@ cdef api SyclEvent SyclEvent_Make(DPCTLSyclEventRef ERef):
     return SyclEvent._create(copied_ERef)
 
 
-cdef void _event_capsule_deleter(object o):
+cdef void _event_capsule_deleter(object o) noexcept:
     cdef DPCTLSyclEventRef ERef = NULL
     if pycapsule.PyCapsule_IsValid(o, "SyclEventRef"):
         ERef = <DPCTLSyclEventRef> pycapsule.PyCapsule_GetPointer(

dpctl/_sycl_queue.pyx

@@ -121,7 +121,7 @@ cdef class SyclAsynchronousError(Exception):
     """
 
 
-cdef void default_async_error_handler(int err) nogil except *:
+cdef void default_async_error_handler(int err) except * nogil:
     with gil:
         raise SyclAsynchronousError(err)
 
@@ -159,7 +159,7 @@ cdef int _parse_queue_properties(object prop) except *:
     return res
 
 
-cdef void _queue_capsule_deleter(object o):
+cdef void _queue_capsule_deleter(object o) noexcept:
     cdef DPCTLSyclQueueRef QRef = NULL
     if pycapsule.PyCapsule_IsValid(o, "SyclQueueRef"):
         QRef = <DPCTLSyclQueueRef> pycapsule.PyCapsule_GetPointer(

dpctl/apis/include/dpctl_capi.h

@@ -28,6 +28,7 @@
 // Ordering of includes is important here. dpctl_sycl_types defines types
 // used by dpctl's Python C-API headers.
 #include "syclinterface/dpctl_sycl_types.h"
+#define CYTHON_EXTERN_C extern "C"
 #include "../_sycl_device.h"
 #include "../_sycl_device_api.h"
 #include "../_sycl_context.h"