make examples free-threading compatible

Author: ndgrigorian

examples/c/py_sycl_ls/src/py_sycl-ls.c

@@ -63,25 +63,35 @@ static PyMethodDef SyclLSMethods[] = {
     {NULL, NULL, 0, NULL} /* Sentinel */
 };
 
+static int syclls_module_exec(PyObject *m)
+{
+    (void)(m);
+    import_dpctl();
+    if (PyErr_Occurred()) {
+        return -1;
+    }
+    return 0;
+}
+
+static PyModuleDef_Slot syclls_module_slots[] = {
+    {Py_mod_exec, syclls_module_exec},
+#if PY_VERSION_HEX >= 0x030D0000
+    {Py_mod_gil, Py_MOD_GIL_NOT_USED},
+#endif
+    {0, NULL}};
+
 static struct PyModuleDef syclls_module = {
     PyModuleDef_HEAD_INIT,
     "_py_sycl_ls", /* name of module */
     "",            /* module documentation, may be NULL */
-    -1,            /* size of per-interpreter state of the module,
-                      or -1 if the module keeps state in global variables. */
+    0,             /* size of per-interpreter state of the module */
     SyclLSMethods,
-    NULL,
+    syclls_module_slots,
     NULL,
     NULL,
     NULL};
 
 PyMODINIT_FUNC PyInit__py_sycl_ls(void)
 {
-    PyObject *m;
-
-    import_dpctl();
-
-    m = PyModule_Create(&syclls_module);
-
-    return m;
+    return PyModuleDef_Init(&syclls_module);
 }

examples/cython/sycl_buffer/syclbuffer/_syclbuffer.pyx

@@ -16,6 +16,7 @@
 
 # distutils: language = c++
 # cython: language_level=3
+# cython: freethreading_compatible = True
 
 cimport cython
 

examples/cython/use_dpctl_sycl/use_dpctl_sycl/_cython_api.pyx

@@ -17,6 +17,7 @@
 # distutils: language = c++
 # cython: language_level=3
 # cython: linetrace=True
+# cython: freethreading_compatible = True
 
 cimport libcpp.string
 

examples/pybind11/external_usm_allocation/external_usm_allocation/_usm_alloc_example.cpp

@@ -141,7 +141,7 @@ dpctl::memory::usm_memory make_zeroed_device_memory(size_t nbytes,
     return dpctl::memory::usm_memory(data, nbytes, q, shptr);
 }
 
-PYBIND11_MODULE(_external_usm_alloc, m)
+PYBIND11_MODULE(_external_usm_alloc, m, py::mod_gil_not_used())
 {
     py::class_<DMatrix> dm(m, "DMatrix");
     dm.def(py::init(&create_matrix),

examples/pybind11/onemkl_gemv/sycl_gemm/_onemkl.cpp

@@ -521,7 +521,7 @@ int py_cg_solve(sycl::queue exec_q,
     }
 }
 
-PYBIND11_MODULE(_onemkl, m)
+PYBIND11_MODULE(_onemkl, m, py::mod_gil_not_used())
 {
     m.def("gemv", &py_gemv, "Uses oneMKL to compute dot(matrix, vector)",
           py::arg("exec_queue"), py::arg("Amatrix"), py::arg("xvec"),

examples/pybind11/use_dpctl_sycl_kernel/use_kernel/_example.cpp

@@ -75,7 +75,7 @@ void submit_custom_kernel(sycl::queue &q,
     return;
 }
 
-PYBIND11_MODULE(_use_kernel, m)
+PYBIND11_MODULE(_use_kernel, m, py::mod_gil_not_used())
 {
     m.def("submit_custom_kernel", &submit_custom_kernel,
           "Submit given kernel with arguments (int *, int *) to queue",

examples/pybind11/use_dpctl_sycl_queue/use_queue_device/_example.cpp

@@ -95,7 +95,7 @@ std::uint32_t get_partition_max_sub_devices(const sycl::device &d)
     return d.get_info<sycl::info::device::partition_max_sub_devices>();
 }
 
-PYBIND11_MODULE(_use_queue_device, m)
+PYBIND11_MODULE(_use_queue_device, m, py::mod_gil_not_used())
 {
     m.def(
         "get_max_compute_units",