diff --git a/cuda_bindings/cuda/bindings/_internal/nvml.pxd b/cuda_bindings/cuda/bindings/_internal/nvml.pxd index eea80739f07..272a77d24db 100644 --- a/cuda_bindings/cuda/bindings/_internal/nvml.pxd +++ b/cuda_bindings/cuda/bindings/_internal/nvml.pxd @@ -4,7 +4,7 @@ # # This code was automatically generated across versions from 12.9.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=ed4c433854399c2e4f1adc3ffcfc37901e1be29c5aa50728498c87225edf92b1 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=c2cc3cd086b5aeea5fad7ca17600d0102691a3cb354b916f5c086c383d77df19 from ..cynvml cimport * @@ -363,3 +363,7 @@ cdef nvmlReturn_t _nvmlDeviceGetVgpuSchedulerLog_v2(nvmlDevice_t device, nvmlVgp cdef nvmlReturn_t _nvmlGpuInstanceGetVgpuSchedulerLog_v2(nvmlGpuInstance_t gpuInstance, nvmlVgpuSchedulerLogInfo_v2_t* pSchedulerLogInfo) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil cdef nvmlReturn_t _nvmlDeviceSetVgpuSchedulerState_v2(nvmlDevice_t device, nvmlVgpuSchedulerState_v2_t* pSchedulerState) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil cdef nvmlReturn_t _nvmlGpuInstanceSetVgpuSchedulerState_v2(nvmlGpuInstance_t gpuInstance, nvmlVgpuSchedulerState_v2_t* pSchedulerState) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil +cdef nvmlReturn_t _nvmlSystemGetCPER_v1(nvmlGetCPER_v1_t* cper) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil +cdef nvmlReturn_t _nvmlDeviceGetBBXTimeData_v1(nvmlDevice_t device, nvmlBBXTimeData_v1_t* timeData) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil +cdef nvmlReturn_t _nvmlDeviceGetAccountingStats_v2(nvmlDevice_t device, nvmlAccountingStats_v2_t* stats) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil +cdef nvmlReturn_t _nvmlDeviceGetRemappedRows_v2(nvmlDevice_t device, nvmlRemappedRowsInfo_v2_t* info) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil diff --git a/cuda_bindings/cuda/bindings/_internal/nvml_linux.pyx b/cuda_bindings/cuda/bindings/_internal/nvml_linux.pyx index d2882b251b0..be534de181d 100644 --- a/cuda_bindings/cuda/bindings/_internal/nvml_linux.pyx +++ b/cuda_bindings/cuda/bindings/_internal/nvml_linux.pyx @@ -3,7 +3,7 @@ # SPDX-License-Identifier: Apache-2.0 # # This code was automatically generated across versions from 12.9.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=646d902675de6987cff08e5702d3b2bff889e6a827273e57413aa5de45a5897a +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=45cd03eeb8717b33a1e11d83ae99ac8d6b580e4c57fad99d185614bd0047faf3 # <<<< PREAMBLE CONTENT >>>> @@ -415,6 +415,10 @@ cdef void* __nvmlDeviceGetVgpuSchedulerLog_v2 = NULL cdef void* __nvmlGpuInstanceGetVgpuSchedulerLog_v2 = NULL cdef void* __nvmlDeviceSetVgpuSchedulerState_v2 = NULL cdef void* __nvmlGpuInstanceSetVgpuSchedulerState_v2 = NULL +cdef void* __nvmlSystemGetCPER_v1 = NULL +cdef void* __nvmlDeviceGetBBXTimeData_v1 = NULL +cdef void* __nvmlDeviceGetAccountingStats_v2 = NULL +cdef void* __nvmlDeviceGetRemappedRows_v2 = NULL cdef int _init_nvml() except -1 nogil: global _cyb___py_nvml_init @@ -2879,6 +2883,34 @@ cdef int _init_nvml() except -1 nogil: handle = load_library() __nvmlGpuInstanceSetVgpuSchedulerState_v2 = _cyb_dlsym(handle, 'nvmlGpuInstanceSetVgpuSchedulerState_v2') + global __nvmlSystemGetCPER_v1 + __nvmlSystemGetCPER_v1 = _cyb_dlsym(_cyb_RTLD_DEFAULT, 'nvmlSystemGetCPER_v1') + if __nvmlSystemGetCPER_v1 == NULL: + if handle == NULL: + handle = load_library() + __nvmlSystemGetCPER_v1 = _cyb_dlsym(handle, 'nvmlSystemGetCPER_v1') + + global __nvmlDeviceGetBBXTimeData_v1 + __nvmlDeviceGetBBXTimeData_v1 = _cyb_dlsym(_cyb_RTLD_DEFAULT, 'nvmlDeviceGetBBXTimeData_v1') + if __nvmlDeviceGetBBXTimeData_v1 == NULL: + if handle == NULL: + handle = load_library() + __nvmlDeviceGetBBXTimeData_v1 = _cyb_dlsym(handle, 'nvmlDeviceGetBBXTimeData_v1') + + global __nvmlDeviceGetAccountingStats_v2 + __nvmlDeviceGetAccountingStats_v2 = _cyb_dlsym(_cyb_RTLD_DEFAULT, 'nvmlDeviceGetAccountingStats_v2') + if __nvmlDeviceGetAccountingStats_v2 == NULL: + if handle == NULL: + handle = load_library() + __nvmlDeviceGetAccountingStats_v2 = _cyb_dlsym(handle, 'nvmlDeviceGetAccountingStats_v2') + + global __nvmlDeviceGetRemappedRows_v2 + __nvmlDeviceGetRemappedRows_v2 = _cyb_dlsym(_cyb_RTLD_DEFAULT, 'nvmlDeviceGetRemappedRows_v2') + if __nvmlDeviceGetRemappedRows_v2 == NULL: + if handle == NULL: + handle = load_library() + __nvmlDeviceGetRemappedRows_v2 = _cyb_dlsym(handle, 'nvmlDeviceGetRemappedRows_v2') + _cyb_atomic_int_store(&_cyb___py_nvml_init, 1) return 0 @@ -3948,6 +3980,18 @@ cpdef dict _inspect_function_pointers(): global __nvmlGpuInstanceSetVgpuSchedulerState_v2 data["__nvmlGpuInstanceSetVgpuSchedulerState_v2"] = <_cyb_intptr_t>__nvmlGpuInstanceSetVgpuSchedulerState_v2 + + global __nvmlSystemGetCPER_v1 + data["__nvmlSystemGetCPER_v1"] = <_cyb_intptr_t>__nvmlSystemGetCPER_v1 + + global __nvmlDeviceGetBBXTimeData_v1 + data["__nvmlDeviceGetBBXTimeData_v1"] = <_cyb_intptr_t>__nvmlDeviceGetBBXTimeData_v1 + + global __nvmlDeviceGetAccountingStats_v2 + data["__nvmlDeviceGetAccountingStats_v2"] = <_cyb_intptr_t>__nvmlDeviceGetAccountingStats_v2 + + global __nvmlDeviceGetRemappedRows_v2 + data["__nvmlDeviceGetRemappedRows_v2"] = <_cyb_intptr_t>__nvmlDeviceGetRemappedRows_v2 _cyb_func_ptrs = data return data @@ -7478,3 +7522,43 @@ cdef nvmlReturn_t _nvmlGpuInstanceSetVgpuSchedulerState_v2(nvmlGpuInstance_t gpu raise FunctionNotFoundError("function nvmlGpuInstanceSetVgpuSchedulerState_v2 is not found") return (__nvmlGpuInstanceSetVgpuSchedulerState_v2)( gpuInstance, pSchedulerState) + + +cdef nvmlReturn_t _nvmlSystemGetCPER_v1(nvmlGetCPER_v1_t* cper) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + global __nvmlSystemGetCPER_v1 + _check_or_init_nvml() + if __nvmlSystemGetCPER_v1 == NULL: + with gil: + raise FunctionNotFoundError("function nvmlSystemGetCPER_v1 is not found") + return (__nvmlSystemGetCPER_v1)( + cper) + + +cdef nvmlReturn_t _nvmlDeviceGetBBXTimeData_v1(nvmlDevice_t device, nvmlBBXTimeData_v1_t* timeData) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + global __nvmlDeviceGetBBXTimeData_v1 + _check_or_init_nvml() + if __nvmlDeviceGetBBXTimeData_v1 == NULL: + with gil: + raise FunctionNotFoundError("function nvmlDeviceGetBBXTimeData_v1 is not found") + return (__nvmlDeviceGetBBXTimeData_v1)( + device, timeData) + + +cdef nvmlReturn_t _nvmlDeviceGetAccountingStats_v2(nvmlDevice_t device, nvmlAccountingStats_v2_t* stats) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + global __nvmlDeviceGetAccountingStats_v2 + _check_or_init_nvml() + if __nvmlDeviceGetAccountingStats_v2 == NULL: + with gil: + raise FunctionNotFoundError("function nvmlDeviceGetAccountingStats_v2 is not found") + return (__nvmlDeviceGetAccountingStats_v2)( + device, stats) + + +cdef nvmlReturn_t _nvmlDeviceGetRemappedRows_v2(nvmlDevice_t device, nvmlRemappedRowsInfo_v2_t* info) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + global __nvmlDeviceGetRemappedRows_v2 + _check_or_init_nvml() + if __nvmlDeviceGetRemappedRows_v2 == NULL: + with gil: + raise FunctionNotFoundError("function nvmlDeviceGetRemappedRows_v2 is not found") + return (__nvmlDeviceGetRemappedRows_v2)( + device, info) diff --git a/cuda_bindings/cuda/bindings/_internal/nvml_windows.pyx b/cuda_bindings/cuda/bindings/_internal/nvml_windows.pyx index f7ae66ae98e..ce46586baf5 100644 --- a/cuda_bindings/cuda/bindings/_internal/nvml_windows.pyx +++ b/cuda_bindings/cuda/bindings/_internal/nvml_windows.pyx @@ -3,7 +3,7 @@ # SPDX-License-Identifier: Apache-2.0 # # This code was automatically generated across versions from 12.9.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=831330186c4a7bb029b953be6dd3cda119a7f10c56fa9378ab621fbc4374f9d1 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=d7b5ba031ed135b60903431812f9883efdd554268990e04003d5ead5674466eb # <<<< PREAMBLE CONTENT >>>> @@ -412,6 +412,10 @@ cdef void* __nvmlDeviceGetVgpuSchedulerLog_v2 = NULL cdef void* __nvmlGpuInstanceGetVgpuSchedulerLog_v2 = NULL cdef void* __nvmlDeviceSetVgpuSchedulerState_v2 = NULL cdef void* __nvmlGpuInstanceSetVgpuSchedulerState_v2 = NULL +cdef void* __nvmlSystemGetCPER_v1 = NULL +cdef void* __nvmlDeviceGetBBXTimeData_v1 = NULL +cdef void* __nvmlDeviceGetAccountingStats_v2 = NULL +cdef void* __nvmlDeviceGetRemappedRows_v2 = NULL cdef int _init_nvml() except -1 nogil: global _cyb___py_nvml_init @@ -1475,6 +1479,18 @@ cdef int _init_nvml() except -1 nogil: global __nvmlGpuInstanceSetVgpuSchedulerState_v2 __nvmlGpuInstanceSetVgpuSchedulerState_v2 = _cyb_GetProcAddress(handle, 'nvmlGpuInstanceSetVgpuSchedulerState_v2') + global __nvmlSystemGetCPER_v1 + __nvmlSystemGetCPER_v1 = _cyb_GetProcAddress(handle, 'nvmlSystemGetCPER_v1') + + global __nvmlDeviceGetBBXTimeData_v1 + __nvmlDeviceGetBBXTimeData_v1 = _cyb_GetProcAddress(handle, 'nvmlDeviceGetBBXTimeData_v1') + + global __nvmlDeviceGetAccountingStats_v2 + __nvmlDeviceGetAccountingStats_v2 = _cyb_GetProcAddress(handle, 'nvmlDeviceGetAccountingStats_v2') + + global __nvmlDeviceGetRemappedRows_v2 + __nvmlDeviceGetRemappedRows_v2 = _cyb_GetProcAddress(handle, 'nvmlDeviceGetRemappedRows_v2') + _cyb_atomic_int_store(&_cyb___py_nvml_init, 1) return 0 @@ -2544,6 +2560,18 @@ cpdef dict _inspect_function_pointers(): global __nvmlGpuInstanceSetVgpuSchedulerState_v2 data["__nvmlGpuInstanceSetVgpuSchedulerState_v2"] = <_cyb_intptr_t>__nvmlGpuInstanceSetVgpuSchedulerState_v2 + + global __nvmlSystemGetCPER_v1 + data["__nvmlSystemGetCPER_v1"] = <_cyb_intptr_t>__nvmlSystemGetCPER_v1 + + global __nvmlDeviceGetBBXTimeData_v1 + data["__nvmlDeviceGetBBXTimeData_v1"] = <_cyb_intptr_t>__nvmlDeviceGetBBXTimeData_v1 + + global __nvmlDeviceGetAccountingStats_v2 + data["__nvmlDeviceGetAccountingStats_v2"] = <_cyb_intptr_t>__nvmlDeviceGetAccountingStats_v2 + + global __nvmlDeviceGetRemappedRows_v2 + data["__nvmlDeviceGetRemappedRows_v2"] = <_cyb_intptr_t>__nvmlDeviceGetRemappedRows_v2 _cyb_func_ptrs = data return data @@ -6073,3 +6101,43 @@ cdef nvmlReturn_t _nvmlGpuInstanceSetVgpuSchedulerState_v2(nvmlGpuInstance_t gpu raise FunctionNotFoundError("function nvmlGpuInstanceSetVgpuSchedulerState_v2 is not found") return (__nvmlGpuInstanceSetVgpuSchedulerState_v2)( gpuInstance, pSchedulerState) + + +cdef nvmlReturn_t _nvmlSystemGetCPER_v1(nvmlGetCPER_v1_t* cper) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + global __nvmlSystemGetCPER_v1 + _check_or_init_nvml() + if __nvmlSystemGetCPER_v1 == NULL: + with gil: + raise FunctionNotFoundError("function nvmlSystemGetCPER_v1 is not found") + return (__nvmlSystemGetCPER_v1)( + cper) + + +cdef nvmlReturn_t _nvmlDeviceGetBBXTimeData_v1(nvmlDevice_t device, nvmlBBXTimeData_v1_t* timeData) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + global __nvmlDeviceGetBBXTimeData_v1 + _check_or_init_nvml() + if __nvmlDeviceGetBBXTimeData_v1 == NULL: + with gil: + raise FunctionNotFoundError("function nvmlDeviceGetBBXTimeData_v1 is not found") + return (__nvmlDeviceGetBBXTimeData_v1)( + device, timeData) + + +cdef nvmlReturn_t _nvmlDeviceGetAccountingStats_v2(nvmlDevice_t device, nvmlAccountingStats_v2_t* stats) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + global __nvmlDeviceGetAccountingStats_v2 + _check_or_init_nvml() + if __nvmlDeviceGetAccountingStats_v2 == NULL: + with gil: + raise FunctionNotFoundError("function nvmlDeviceGetAccountingStats_v2 is not found") + return (__nvmlDeviceGetAccountingStats_v2)( + device, stats) + + +cdef nvmlReturn_t _nvmlDeviceGetRemappedRows_v2(nvmlDevice_t device, nvmlRemappedRowsInfo_v2_t* info) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + global __nvmlDeviceGetRemappedRows_v2 + _check_or_init_nvml() + if __nvmlDeviceGetRemappedRows_v2 == NULL: + with gil: + raise FunctionNotFoundError("function nvmlDeviceGetRemappedRows_v2 is not found") + return (__nvmlDeviceGetRemappedRows_v2)( + device, info) diff --git a/cuda_bindings/cuda/bindings/cufile.pyx b/cuda_bindings/cuda/bindings/cufile.pyx index fbc9c20dc47..eb892e41535 100644 --- a/cuda_bindings/cuda/bindings/cufile.pyx +++ b/cuda_bindings/cuda/bindings/cufile.pyx @@ -3,7 +3,7 @@ # SPDX-License-Identifier: Apache-2.0 # # This code was automatically generated across versions from 12.9.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=4567ca64d02631fc8d6ed11af8164d72c86b4686c105fd733d186e6c92512749 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=9d2dd7c2d58ea1571aa5e0c4b88a498247727395a9d6864e66abef567efa41ff # <<<< PREAMBLE CONTENT >>>> @@ -2876,10 +2876,12 @@ cpdef intptr_t handle_register(intptr_t descr) except? 0: """cuFileHandleRegister is required, and performs extra checking that is memoized to provide increased performance on later cuFile operations. Args: - descr (intptr_t): ``CUfileDescr_t`` file descriptor (OS agnostic). + descr (intptr_t): ``CUfileDescr_t`` file descriptor (OS + agnostic). Returns: - intptr_t: ``CUfileHandle_t`` opaque file handle for IO operations. + intptr_t: ``CUfileHandle_t`` opaque file handle for IO + operations. .. seealso:: `cuFileHandleRegister` """ @@ -2907,7 +2909,8 @@ cpdef buf_register(intptr_t buf_ptr_base, size_t length, int flags): Args: buf_ptr_base (intptr_t): buffer pointer allocated. - length (size_t): size of memory region from the above specified bufPtr. + length (size_t): size of memory region from the above + specified bufPtr. flags (int): CU_FILE_RDMA_REGISTER. .. seealso:: `cuFileBufRegister` @@ -2967,8 +2970,10 @@ cpdef driver_set_poll_mode(bint poll, size_t poll_threshold_size): """Sets whether the Read/Write APIs use polling to do IO operations This takes place before the driver is opened. No-op if driver is already open. Args: - poll (bint): boolean to indicate whether to use poll mode or not. - poll_threshold_size (size_t): max IO size to use for POLLING mode in KB. + poll (bint): boolean to indicate whether to use poll mode or + not. + poll_threshold_size (size_t): max IO size to use for POLLING + mode in KB. .. seealso:: `cuFileDriverSetPollMode` """ @@ -2981,7 +2986,8 @@ cpdef driver_set_max_direct_io_size(size_t max_direct_io_size): """Control parameter to set max IO size(KB) used by the library to talk to nvidia-fs driver This takes place before the driver is opened. No-op if driver is already open. Args: - max_direct_io_size (size_t): maximum allowed direct io size in KB. + max_direct_io_size (size_t): maximum allowed direct io size in + KB. .. seealso:: `cuFileDriverSetMaxDirectIOSize` """ @@ -2994,7 +3000,8 @@ cpdef driver_set_max_cache_size(size_t max_cache_size): """Control parameter to set maximum GPU memory reserved per device by the library for internal buffering This takes place before the driver is opened. No-op if driver is already open. Args: - max_cache_size (size_t): The maximum GPU buffer space per device used for internal use in KB. + max_cache_size (size_t): The maximum GPU buffer space per + device used for internal use in KB. .. seealso:: `cuFileDriverSetMaxCacheSize` """ @@ -3007,7 +3014,8 @@ cpdef driver_set_max_pinned_mem_size(size_t max_pinned_size): """Sets maximum buffer space that is pinned in KB for use by ``cuFileBufRegister`` This takes place before the driver is opened. No-op if driver is already open. Args: - max_pinned_size (size_t): maximum buffer space that is pinned in KB. + max_pinned_size (size_t): maximum buffer space that is pinned + in KB. .. seealso:: `cuFileDriverSetMaxPinnedMemSize` """ @@ -3133,7 +3141,8 @@ cpdef tuple get_parameter_min_max_value(int param): """Get both the minimum and maximum settable values for a given size_t parameter in a single call. Args: - param (SizeTConfigParameter): CUfile SizeT configuration parameter. + param (SizeTConfigParameter): CUfile SizeT configuration + parameter. Returns: A 2-tuple containing: @@ -3155,7 +3164,8 @@ cpdef set_stats_level(int level): """Set the level of statistics collection for cuFile operations. This will override the cufile.json settings for stats. Args: - level (int): Statistics level (0 = disabled, 1 = basic, 2 = detailed, 3 = verbose). + level (int): Statistics level (0 = disabled, 1 = basic, 2 = + detailed, 3 = verbose). .. seealso:: `cuFileSetStatsLevel` """ @@ -3213,7 +3223,8 @@ cpdef get_stats_l1(intptr_t stats): """Get Level 1 cuFile statistics. Args: - stats (intptr_t): Pointer to ``CUfileStatsLevel1_t`` structure to be filled. + stats (intptr_t): Pointer to ``CUfileStatsLevel1_t`` structure + to be filled. .. seealso:: `cuFileGetStatsL1` """ @@ -3226,7 +3237,8 @@ cpdef get_stats_l2(intptr_t stats): """Get Level 2 cuFile statistics. Args: - stats (intptr_t): Pointer to ``CUfileStatsLevel2_t`` structure to be filled. + stats (intptr_t): Pointer to ``CUfileStatsLevel2_t`` structure + to be filled. .. seealso:: `cuFileGetStatsL2` """ @@ -3239,7 +3251,8 @@ cpdef get_stats_l3(intptr_t stats): """Get Level 3 cuFile statistics. Args: - stats (intptr_t): Pointer to ``CUfileStatsLevel3_t`` structure to be filled. + stats (intptr_t): Pointer to ``CUfileStatsLevel3_t`` structure + to be filled. .. seealso:: `cuFileGetStatsL3` """ @@ -3277,7 +3290,8 @@ cpdef get_parameter_posix_pool_slab_array(intptr_t size_values, intptr_t count_v Args: size_values (intptr_t): Buffer to receive slab sizes in KB. count_values (intptr_t): Buffer to receive slab counts. - len (int): Buffer size (must match the actual parameter length). + len (int): Buffer size (must match the actual parameter + length). .. seealso:: `cuFileGetParameterPosixPoolSlabArray` """ @@ -3346,4 +3360,6 @@ cpdef write(intptr_t fh, intptr_t buf_ptr_base, size_t size, off_t file_offset, status = cuFileWrite(fh, buf_ptr_base, size, file_offset, buf_ptr_offset) check_status(status) return status + + del _cyb_FastEnum diff --git a/cuda_bindings/cuda/bindings/cydriver.pxd b/cuda_bindings/cuda/bindings/cydriver.pxd index 43f9d031e24..cde96a903c2 100644 --- a/cuda_bindings/cuda/bindings/cydriver.pxd +++ b/cuda_bindings/cuda/bindings/cydriver.pxd @@ -4,7 +4,7 @@ # # This code was automatically generated across versions from 12.9.0 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=cccb0572002cd20232f2b9f5c7acf559c92813d33dfc364136d57c8f453e50c6 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=3d716616a92d8ac919b59eccac24b84cb45d655dfb75436b7f9714c71d6f39e6 from libc.stdint cimport uint32_t, uint64_t @@ -3716,6 +3716,7 @@ cdef enum: CU_MEM_CREATE_USAGE_TILE_POOL = 1 cdef enum: CU_MEM_CREATE_USAGE_HW_DECOMPRESS = 2 + cdef enum: CU_MEM_POOL_CREATE_USAGE_HW_DECOMPRESS = 2 cdef enum: CUDA_COOPERATIVE_LAUNCH_MULTI_DEVICE_NO_PRE_LAUNCH_SYNC = 1 diff --git a/cuda_bindings/cuda/bindings/cynvml.pxd b/cuda_bindings/cuda/bindings/cynvml.pxd index 61ac3fa0da7..59d2d8286d6 100644 --- a/cuda_bindings/cuda/bindings/cynvml.pxd +++ b/cuda_bindings/cuda/bindings/cynvml.pxd @@ -4,7 +4,7 @@ # # This code was automatically generated across versions from 12.9.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=5e55307c8ff89e076c29fc7c2a36bf0af7ecf3162693a4c94d7fca65454d6a9e +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=f4f48bbdecd36a33b5561334a2c33ce79322a49091f8ac6cfea40ec71c94287a from libc.stdint cimport int64_t @@ -2357,3 +2357,7 @@ cdef nvmlReturn_t nvmlDeviceGetVgpuSchedulerLog_v2(nvmlDevice_t device, nvmlVgpu cdef nvmlReturn_t nvmlGpuInstanceGetVgpuSchedulerLog_v2(nvmlGpuInstance_t gpuInstance, nvmlVgpuSchedulerLogInfo_v2_t* pSchedulerLogInfo) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil cdef nvmlReturn_t nvmlDeviceSetVgpuSchedulerState_v2(nvmlDevice_t device, nvmlVgpuSchedulerState_v2_t* pSchedulerState) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil cdef nvmlReturn_t nvmlGpuInstanceSetVgpuSchedulerState_v2(nvmlGpuInstance_t gpuInstance, nvmlVgpuSchedulerState_v2_t* pSchedulerState) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil +cdef nvmlReturn_t nvmlSystemGetCPER_v1(nvmlGetCPER_v1_t* cper) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil +cdef nvmlReturn_t nvmlDeviceGetBBXTimeData_v1(nvmlDevice_t device, nvmlBBXTimeData_v1_t* timeData) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil +cdef nvmlReturn_t nvmlDeviceGetAccountingStats_v2(nvmlDevice_t device, nvmlAccountingStats_v2_t* stats) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil +cdef nvmlReturn_t nvmlDeviceGetRemappedRows_v2(nvmlDevice_t device, nvmlRemappedRowsInfo_v2_t* info) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil diff --git a/cuda_bindings/cuda/bindings/cynvml.pyx b/cuda_bindings/cuda/bindings/cynvml.pyx index 612368c7736..9b2f7df7c54 100644 --- a/cuda_bindings/cuda/bindings/cynvml.pyx +++ b/cuda_bindings/cuda/bindings/cynvml.pyx @@ -4,7 +4,7 @@ # # This code was automatically generated across versions from 12.9.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=ec221879a459b2de9b3dfe54cba58613e9c08b279a95f782a450c98fd7cea532 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=b30ca4e9dfac73d38cb872e4dc7d80d69cbb7e516c50e048cb34234a6c0198a6 from ._internal cimport nvml as _nvml @@ -1414,3 +1414,19 @@ cdef nvmlReturn_t nvmlDeviceSetVgpuSchedulerState_v2(nvmlDevice_t device, nvmlVg cdef nvmlReturn_t nvmlGpuInstanceSetVgpuSchedulerState_v2(nvmlGpuInstance_t gpuInstance, nvmlVgpuSchedulerState_v2_t* pSchedulerState) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: return _nvml._nvmlGpuInstanceSetVgpuSchedulerState_v2(gpuInstance, pSchedulerState) + + +cdef nvmlReturn_t nvmlSystemGetCPER_v1(nvmlGetCPER_v1_t* cper) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + return _nvml._nvmlSystemGetCPER_v1(cper) + + +cdef nvmlReturn_t nvmlDeviceGetBBXTimeData_v1(nvmlDevice_t device, nvmlBBXTimeData_v1_t* timeData) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + return _nvml._nvmlDeviceGetBBXTimeData_v1(device, timeData) + + +cdef nvmlReturn_t nvmlDeviceGetAccountingStats_v2(nvmlDevice_t device, nvmlAccountingStats_v2_t* stats) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + return _nvml._nvmlDeviceGetAccountingStats_v2(device, stats) + + +cdef nvmlReturn_t nvmlDeviceGetRemappedRows_v2(nvmlDevice_t device, nvmlRemappedRowsInfo_v2_t* info) except?_NVMLRETURN_T_INTERNAL_LOADING_ERROR nogil: + return _nvml._nvmlDeviceGetRemappedRows_v2(device, info) diff --git a/cuda_bindings/cuda/bindings/cyruntime.pxd b/cuda_bindings/cuda/bindings/cyruntime.pxd index 58e0a14ca60..7eb76712237 100644 --- a/cuda_bindings/cuda/bindings/cyruntime.pxd +++ b/cuda_bindings/cuda/bindings/cyruntime.pxd @@ -4,7 +4,7 @@ # # This code was automatically generated across versions from 12.9.0 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=2b62a3b56226f5cf6953f578057af792369a100b7775328c5aa66d81d780d2ac +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=a7205ec1f1749acd8f9e32e85660d77d8ccb60a0d038bb63fb4b015496f23d07 from libc.stdint cimport uint32_t, uint64_t @@ -1254,6 +1254,20 @@ cdef extern from 'library_types.h': CUDA_EMULATION_STRATEGY_EAGER ctypedef cudaEmulationStrategy_t cudaEmulationStrategy +cdef extern from 'library_types.h': + cdef enum cudaEmulationMantissaControl_t: + CUDA_EMULATION_MANTISSA_CONTROL_DYNAMIC + CUDA_EMULATION_MANTISSA_CONTROL_FIXED + ctypedef cudaEmulationMantissaControl_t cudaEmulationMantissaControl + +cdef extern from 'library_types.h': + cdef enum cudaEmulationSpecialValuesSupport_t: + CUDA_EMULATION_SPECIAL_VALUES_SUPPORT_DEFAULT + CUDA_EMULATION_SPECIAL_VALUES_SUPPORT_NONE + CUDA_EMULATION_SPECIAL_VALUES_SUPPORT_INFINITY + CUDA_EMULATION_SPECIAL_VALUES_SUPPORT_NAN + ctypedef cudaEmulationSpecialValuesSupport_t cudaEmulationSpecialValuesSupport + cdef extern from 'driver_types.h': cdef enum cudaDevSmResourceGroup_flags: cudaDevSmResourceGroupDefault @@ -1276,20 +1290,6 @@ cdef extern from 'driver_types.h': cudaDevWorkqueueConfigScopeDeviceCtx cudaDevWorkqueueConfigScopeGreenCtxBalanced -cdef extern from 'library_types.h': - cdef enum cudaEmulationMantissaControl_t: - CUDA_EMULATION_MANTISSA_CONTROL_DYNAMIC - CUDA_EMULATION_MANTISSA_CONTROL_FIXED - ctypedef cudaEmulationMantissaControl_t cudaEmulationMantissaControl - -cdef extern from 'library_types.h': - cdef enum cudaEmulationSpecialValuesSupport_t: - CUDA_EMULATION_SPECIAL_VALUES_SUPPORT_DEFAULT - CUDA_EMULATION_SPECIAL_VALUES_SUPPORT_NONE - CUDA_EMULATION_SPECIAL_VALUES_SUPPORT_INFINITY - CUDA_EMULATION_SPECIAL_VALUES_SUPPORT_NAN - ctypedef cudaEmulationSpecialValuesSupport_t cudaEmulationSpecialValuesSupport - cdef extern from 'driver_types.h': cdef enum cudaHostTaskSyncMode: cudaHostTaskBlocking diff --git a/cuda_bindings/cuda/bindings/driver.pxd b/cuda_bindings/cuda/bindings/driver.pxd index 9f4d912a3c4..8c5e32e0f65 100644 --- a/cuda_bindings/cuda/bindings/driver.pxd +++ b/cuda_bindings/cuda/bindings/driver.pxd @@ -2,7 +2,7 @@ # SPDX-License-Identifier: Apache-2.0 # This code was automatically generated with version 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=f4b08b7f4b26966f9f462562819700500a100748c5b34ab47de79836e6bec3f2 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=3559a38253c9137d67c5955419f694d32429a7355b84c6e7e06ba1d43a296193 cimport cuda.bindings.cydriver as cydriver include "_lib/utils.pxd" @@ -545,13 +545,6 @@ cdef class CUipcEventHandle_st: """ CUDA IPC event handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -564,13 +557,6 @@ cdef class CUipcMemHandle_st: """ CUDA IPC mem handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -1538,11 +1524,6 @@ cdef class CUgraphEdgeData_st: See CUgraphDependencyType. - reserved : bytes - These bytes are unused and must be zeroed. This ensures - compatibility if additional fields are added in the future. - - Methods ------- getPtr() @@ -2336,10 +2317,6 @@ cdef class CUDA_MEMCPY3D_st: Source array reference - reserved0 : Any - Must be NULL - - srcPitch : size_t Source pitch (ignored when src is array) @@ -2380,10 +2357,6 @@ cdef class CUDA_MEMCPY3D_st: Destination array reference - reserved1 : Any - Must be NULL - - dstPitch : size_t Destination pitch (ignored when dst is array) @@ -2422,9 +2395,6 @@ cdef class CUDA_MEMCPY3D_st: cdef CUarray _srcArray - cdef _HelperInputVoidPtr _cyreserved0 - - cdef _HelperInputVoidPtr _cydstHost @@ -2434,9 +2404,6 @@ cdef class CUDA_MEMCPY3D_st: cdef CUarray _dstArray - cdef _HelperInputVoidPtr _cyreserved1 - - cdef class CUDA_MEMCPY3D_PEER_st: """ 3D memory cross-context copy parameters @@ -2589,10 +2556,6 @@ cdef class CUDA_MEMCPY_NODE_PARAMS_st: Must be zero - reserved : int - Must be zero - - copyCtx : CUcontext Context on which to run the node @@ -2733,10 +2696,6 @@ cdef class CUDA_ARRAY_SPARSE_PROPERTIES_st: CU_ARRAY_SPARSE_PROPERTIES_SINGLE_MIPTAIL - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -2763,10 +2722,6 @@ cdef class CUDA_ARRAY_MEMORY_REQUIREMENTS_st: alignment requirement - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -2885,13 +2840,6 @@ cdef class anon_struct10: cdef class anon_struct11: """ - Attributes - ---------- - - reserved : list[int] - - - Methods ------- getPtr() @@ -2920,10 +2868,6 @@ cdef class anon_union4: - reserved : anon_struct11 - - - Methods ------- getPtr() @@ -2943,9 +2887,6 @@ cdef class anon_union4: cdef anon_struct10 _pitch2D - cdef anon_struct11 _reserved - - cdef class CUDA_RESOURCE_DESC_st: """ CUDA Resource descriptor @@ -3019,10 +2960,6 @@ cdef class CUDA_TEXTURE_DESC_st: Border Color - reserved : list[int] - - - Methods ------- getPtr() @@ -3070,10 +3007,6 @@ cdef class CUDA_RESOURCE_VIEW_DESC_st: Last layer index - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -3268,10 +3201,6 @@ cdef class CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st: Flags must either be zero or CUDA_EXTERNAL_MEMORY_DEDICATED - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -3302,10 +3231,6 @@ cdef class CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st: Flags reserved for future use. Must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -3334,10 +3259,6 @@ cdef class CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st: Total number of levels in the mipmap chain - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -3424,10 +3345,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st: Flags reserved for the future. Must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -3464,10 +3381,6 @@ cdef class anon_union7: - reserved : unsigned long long - - - Methods ------- getPtr() @@ -3511,10 +3424,6 @@ cdef class anon_struct16: - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -3553,10 +3462,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st: For all other types of CUexternalSemaphore, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -3593,10 +3498,6 @@ cdef class anon_union8: - reserved : unsigned long long - - - Methods ------- getPtr() @@ -3644,10 +3545,6 @@ cdef class anon_struct19: - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -3686,10 +3583,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st: For all other types of CUexternalSemaphore, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -4032,10 +3925,6 @@ cdef class CUarrayMapInfo_st: flags for future use, must be zero now. - reserved : list[unsigned int] - Reserved for future use, must be zero now. - - Methods ------- getPtr() @@ -4095,10 +3984,6 @@ cdef class anon_struct22: - reserved : bytes - - - Methods ------- getPtr() @@ -4287,10 +4172,6 @@ cdef class CUmemPoolProps_st: Bitmask indicating intended usage for the pool. - reserved : bytes - reserved for future use, must be 0 - - Methods ------- getPtr() @@ -4309,13 +4190,6 @@ cdef class CUmemPoolPtrExportData_st: """ Opaque data for exporting a pool allocation - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -4779,14 +4653,6 @@ cdef class CUgraphNodeParams_st: Type of the node - reserved0 : list[int] - Reserved. Must be zero. - - - reserved1 : list[long long] - Padding. Unused bytes must be zero. - - kernel : CUDA_KERNEL_NODE_PARAMS_v3 Kernel node parameters. @@ -4843,10 +4709,6 @@ cdef class CUgraphNodeParams_st: Padding as bytes - reserved2 : long long - Reserved bytes. Must be zero. - - Methods ------- getPtr() @@ -4906,14 +4768,6 @@ cdef class CUcheckpointLockArgs_st: no timeout - reserved0 : unsigned int - Reserved for future use, must be zero - - - reserved1 : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -4926,13 +4780,6 @@ cdef class CUcheckpointCheckpointArgs_st: """ CUDA checkpoint optional checkpoint arguments - Attributes - ---------- - - reserved : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -4986,14 +4833,6 @@ cdef class CUcheckpointRestoreArgs_st: Number of gpu pairs to remap - reserved : bytes - Reserved for future use, must be zeroed - - - reserved : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -5010,13 +4849,6 @@ cdef class CUcheckpointUnlockArgs_st: """ CUDA checkpoint optional unlock arguments - Attributes - ---------- - - reserved : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -5066,10 +4898,6 @@ cdef class CUmemDecompressParams_st: The decompression algorithm to use. - padding : bytes - - - Methods ------- getPtr() @@ -5248,13 +5076,6 @@ cdef class CUdevWorkqueueConfigResource_st: cdef class CUdevWorkqueueResource_st: """ - Attributes - ---------- - - reserved : bytes - Reserved for future use - - Methods ------- getPtr() @@ -5287,10 +5108,6 @@ cdef class CU_DEV_SM_RESOURCE_GROUP_PARAMS_st: CUdevSmResourceGroup_flags. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -5565,13 +5382,6 @@ cdef class CUipcEventHandle_v1(CUipcEventHandle_st): """ CUDA IPC event handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -5583,13 +5393,6 @@ cdef class CUipcEventHandle(CUipcEventHandle_v1): """ CUDA IPC event handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -5601,13 +5404,6 @@ cdef class CUipcMemHandle_v1(CUipcMemHandle_st): """ CUDA IPC mem handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -5619,13 +5415,6 @@ cdef class CUipcMemHandle(CUipcMemHandle_v1): """ CUDA IPC mem handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -6509,11 +6298,6 @@ cdef class CUgraphEdgeData(CUgraphEdgeData_st): See CUgraphDependencyType. - reserved : bytes - These bytes are unused and must be zeroed. This ensures - compatibility if additional fields are added in the future. - - Methods ------- getPtr() @@ -7702,10 +7486,6 @@ cdef class CUDA_MEMCPY3D_v2(CUDA_MEMCPY3D_st): Source array reference - reserved0 : Any - Must be NULL - - srcPitch : size_t Source pitch (ignored when src is array) @@ -7746,10 +7526,6 @@ cdef class CUDA_MEMCPY3D_v2(CUDA_MEMCPY3D_st): Destination array reference - reserved1 : Any - Must be NULL - - dstPitch : size_t Destination pitch (ignored when dst is array) @@ -7817,10 +7593,6 @@ cdef class CUDA_MEMCPY3D(CUDA_MEMCPY3D_v2): Source array reference - reserved0 : Any - Must be NULL - - srcPitch : size_t Source pitch (ignored when src is array) @@ -7861,10 +7633,6 @@ cdef class CUDA_MEMCPY3D(CUDA_MEMCPY3D_v2): Destination array reference - reserved1 : Any - Must be NULL - - dstPitch : size_t Destination pitch (ignored when dst is array) @@ -8136,10 +7904,6 @@ cdef class CUDA_MEMCPY_NODE_PARAMS(CUDA_MEMCPY_NODE_PARAMS_st): Must be zero - reserved : int - Must be zero - - copyCtx : CUcontext Context on which to run the node @@ -8315,10 +8079,6 @@ cdef class CUDA_ARRAY_SPARSE_PROPERTIES_v1(CUDA_ARRAY_SPARSE_PROPERTIES_st): CU_ARRAY_SPARSE_PROPERTIES_SINGLE_MIPTAIL - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8350,10 +8110,6 @@ cdef class CUDA_ARRAY_SPARSE_PROPERTIES(CUDA_ARRAY_SPARSE_PROPERTIES_v1): CU_ARRAY_SPARSE_PROPERTIES_SINGLE_MIPTAIL - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8376,10 +8132,6 @@ cdef class CUDA_ARRAY_MEMORY_REQUIREMENTS_v1(CUDA_ARRAY_MEMORY_REQUIREMENTS_st): alignment requirement - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8402,10 +8154,6 @@ cdef class CUDA_ARRAY_MEMORY_REQUIREMENTS(CUDA_ARRAY_MEMORY_REQUIREMENTS_v1): alignment requirement - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8508,10 +8256,6 @@ cdef class CUDA_TEXTURE_DESC_v1(CUDA_TEXTURE_DESC_st): Border Color - reserved : list[int] - - - Methods ------- getPtr() @@ -8562,10 +8306,6 @@ cdef class CUDA_TEXTURE_DESC(CUDA_TEXTURE_DESC_v1): Border Color - reserved : list[int] - - - Methods ------- getPtr() @@ -8612,10 +8352,6 @@ cdef class CUDA_RESOURCE_VIEW_DESC_v1(CUDA_RESOURCE_VIEW_DESC_st): Last layer index - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8662,10 +8398,6 @@ cdef class CUDA_RESOURCE_VIEW_DESC(CUDA_RESOURCE_VIEW_DESC_v1): Last layer index - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8867,10 +8599,6 @@ cdef class CUDA_EXTERNAL_MEMORY_HANDLE_DESC_v1(CUDA_EXTERNAL_MEMORY_HANDLE_DESC_ Flags must either be zero or CUDA_EXTERNAL_MEMORY_DEDICATED - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8901,10 +8629,6 @@ cdef class CUDA_EXTERNAL_MEMORY_HANDLE_DESC(CUDA_EXTERNAL_MEMORY_HANDLE_DESC_v1) Flags must either be zero or CUDA_EXTERNAL_MEMORY_DEDICATED - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8931,10 +8655,6 @@ cdef class CUDA_EXTERNAL_MEMORY_BUFFER_DESC_v1(CUDA_EXTERNAL_MEMORY_BUFFER_DESC_ Flags reserved for future use. Must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8961,10 +8681,6 @@ cdef class CUDA_EXTERNAL_MEMORY_BUFFER_DESC(CUDA_EXTERNAL_MEMORY_BUFFER_DESC_v1) Flags reserved for future use. Must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8992,10 +8708,6 @@ cdef class CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_v1(CUDA_EXTERNAL_MEMORY_MIP Total number of levels in the mipmap chain - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -9023,10 +8735,6 @@ cdef class CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC(CUDA_EXTERNAL_MEMORY_MIPMAP Total number of levels in the mipmap chain - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -9053,10 +8761,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_v1(CUDA_EXTERNAL_SEMAPHORE_HANDLE Flags reserved for the future. Must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -9083,10 +8787,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC(CUDA_EXTERNAL_SEMAPHORE_HANDLE_DE Flags reserved for the future. Must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -9116,10 +8816,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_v1(CUDA_EXTERNAL_SEMAPHORE_SIGN For all other types of CUexternalSemaphore, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -9149,10 +8845,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS(CUDA_EXTERNAL_SEMAPHORE_SIGNAL_ For all other types of CUexternalSemaphore, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -9182,10 +8874,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_v1(CUDA_EXTERNAL_SEMAPHORE_WAIT_P For all other types of CUexternalSemaphore, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -9215,10 +8903,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS(CUDA_EXTERNAL_SEMAPHORE_WAIT_PARA For all other types of CUexternalSemaphore, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -9448,10 +9132,6 @@ cdef class CUarrayMapInfo_v1(CUarrayMapInfo_st): flags for future use, must be zero now. - reserved : list[unsigned int] - Reserved for future use, must be zero now. - - Methods ------- getPtr() @@ -9507,10 +9187,6 @@ cdef class CUarrayMapInfo(CUarrayMapInfo_v1): flags for future use, must be zero now. - reserved : list[unsigned int] - Reserved for future use, must be zero now. - - Methods ------- getPtr() @@ -9847,10 +9523,6 @@ cdef class CUmemPoolProps_v1(CUmemPoolProps_st): Bitmask indicating intended usage for the pool. - reserved : bytes - reserved for future use, must be 0 - - Methods ------- getPtr() @@ -9895,10 +9567,6 @@ cdef class CUmemPoolProps(CUmemPoolProps_v1): Bitmask indicating intended usage for the pool. - reserved : bytes - reserved for future use, must be 0 - - Methods ------- getPtr() @@ -9910,13 +9578,6 @@ cdef class CUmemPoolPtrExportData_v1(CUmemPoolPtrExportData_st): """ Opaque data for exporting a pool allocation - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -9928,13 +9589,6 @@ cdef class CUmemPoolPtrExportData(CUmemPoolPtrExportData_v1): """ Opaque data for exporting a pool allocation - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -10429,14 +10083,6 @@ cdef class CUgraphNodeParams(CUgraphNodeParams_st): Type of the node - reserved0 : list[int] - Reserved. Must be zero. - - - reserved1 : list[long long] - Padding. Unused bytes must be zero. - - kernel : CUDA_KERNEL_NODE_PARAMS_v3 Kernel node parameters. @@ -10493,10 +10139,6 @@ cdef class CUgraphNodeParams(CUgraphNodeParams_st): Padding as bytes - reserved2 : long long - Reserved bytes. Must be zero. - - Methods ------- getPtr() @@ -10516,14 +10158,6 @@ cdef class CUcheckpointLockArgs(CUcheckpointLockArgs_st): no timeout - reserved0 : unsigned int - Reserved for future use, must be zero - - - reserved1 : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -10535,13 +10169,6 @@ cdef class CUcheckpointCheckpointArgs(CUcheckpointCheckpointArgs_st): """ CUDA checkpoint optional checkpoint arguments - Attributes - ---------- - - reserved : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -10587,14 +10214,6 @@ cdef class CUcheckpointRestoreArgs(CUcheckpointRestoreArgs_st): Number of gpu pairs to remap - reserved : bytes - Reserved for future use, must be zeroed - - - reserved : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -10606,13 +10225,6 @@ cdef class CUcheckpointUnlockArgs(CUcheckpointUnlockArgs_st): """ CUDA checkpoint optional unlock arguments - Attributes - ---------- - - reserved : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -10661,10 +10273,6 @@ cdef class CUmemDecompressParams(CUmemDecompressParams_st): The decompression algorithm to use. - padding : bytes - - - Methods ------- getPtr() @@ -10800,13 +10408,6 @@ cdef class CUdevWorkqueueConfigResource(CUdevWorkqueueConfigResource_st): cdef class CUdevWorkqueueResource(CUdevWorkqueueResource_st): """ - Attributes - ---------- - - reserved : bytes - Reserved for future use - - Methods ------- getPtr() @@ -10838,10 +10439,6 @@ cdef class CU_DEV_SM_RESOURCE_GROUP_PARAMS(CU_DEV_SM_RESOURCE_GROUP_PARAMS_st): CUdevSmResourceGroup_flags. - reserved : list[unsigned int] - - - Methods ------- getPtr() diff --git a/cuda_bindings/cuda/bindings/driver.pyx b/cuda_bindings/cuda/bindings/driver.pyx index 44b7c4c567c..9ede39b83f5 100644 --- a/cuda_bindings/cuda/bindings/driver.pyx +++ b/cuda_bindings/cuda/bindings/driver.pyx @@ -2,7 +2,7 @@ # SPDX-License-Identifier: Apache-2.0 # This code was automatically generated with version 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=4a70be46627269cff03a2b89504463158d6e50d738cfde91e8c3ed1bf88fd9e0 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=d7184de3c786c2c99763253412e592ccda9049dcf4df535a4f7c56effd840435 from typing import Any, Optional import cython import ctypes @@ -9724,13 +9724,6 @@ cdef class CUipcEventHandle_st: """ CUDA IPC event handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -9751,45 +9744,14 @@ cdef class CUipcEventHandle_st: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 64) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 64: - raise ValueError("reserved length must be 64, is " + str(len(reserved))) - if CHAR_MIN == 0: - for i, b in enumerate(reserved): - if b < 0 and b > -129: - b = b + 256 - self._pvt_ptr[0].reserved[i] = b - else: - for i, b in enumerate(reserved): - if b > 127 and b < 256: - b = b - 256 - self._pvt_ptr[0].reserved[i] = b - - cdef class CUipcMemHandle_st: """ CUDA IPC mem handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -9810,34 +9772,10 @@ cdef class CUipcMemHandle_st: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 64) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 64: - raise ValueError("reserved length must be 64, is " + str(len(reserved))) - if CHAR_MIN == 0: - for i, b in enumerate(reserved): - if b < 0 and b > -129: - b = b + 256 - self._pvt_ptr[0].reserved[i] = b - else: - for i, b in enumerate(reserved): - if b > 127 and b < 256: - b = b - 256 - self._pvt_ptr[0].reserved[i] = b - - cdef class CUstreamMemOpWaitValueParams_st: """ Attributes @@ -12977,11 +12915,6 @@ cdef class CUgraphEdgeData_st: See CUgraphDependencyType. - reserved : bytes - These bytes are unused and must be zeroed. This ensures - compatibility if additional fields are added in the future. - - Methods ------- getPtr() @@ -13019,12 +12952,6 @@ cdef class CUgraphEdgeData_st: except ValueError: str_list += ['type : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -13053,17 +12980,6 @@ cdef class CUgraphEdgeData_st: self._pvt_ptr[0].type = type - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 5) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 5: - raise ValueError("reserved length must be 5, is " + str(len(reserved))) - for i, b in enumerate(reserved): - self._pvt_ptr[0].reserved[i] = b - - cdef class CUDA_GRAPH_INSTANTIATE_PARAMS_st: """ Graph instantiation parameters @@ -15433,10 +15349,6 @@ cdef class CUDA_MEMCPY3D_st: Source array reference - reserved0 : Any - Must be NULL - - srcPitch : size_t Source pitch (ignored when src is array) @@ -15477,10 +15389,6 @@ cdef class CUDA_MEMCPY3D_st: Destination array reference - reserved1 : Any - Must be NULL - - dstPitch : size_t Destination pitch (ignored when dst is array) @@ -15582,12 +15490,6 @@ cdef class CUDA_MEMCPY3D_st: str_list += ['srcArray : '] - try: - str_list += ['reserved0 : ' + hex(self.reserved0)] - except ValueError: - str_list += ['reserved0 : '] - - try: str_list += ['srcPitch : ' + str(self.srcPitch)] except ValueError: @@ -15648,12 +15550,6 @@ cdef class CUDA_MEMCPY3D_st: str_list += ['dstArray : '] - try: - str_list += ['reserved1 : ' + hex(self.reserved1)] - except ValueError: - str_list += ['reserved1 : '] - - try: str_list += ['dstPitch : ' + str(self.dstPitch)] except ValueError: @@ -15771,15 +15667,6 @@ cdef class CUDA_MEMCPY3D_st: self._srcArray._pvt_ptr[0] = cysrcArray - @property - def reserved0(self): - return self._pvt_ptr[0].reserved0 - @reserved0.setter - def reserved0(self, reserved0): - self._cyreserved0 = _HelperInputVoidPtr(reserved0) - self._pvt_ptr[0].reserved0 = self._cyreserved0.cptr - - @property def srcPitch(self): return self._pvt_ptr[0].srcPitch @@ -15880,15 +15767,6 @@ cdef class CUDA_MEMCPY3D_st: self._dstArray._pvt_ptr[0] = cydstArray - @property - def reserved1(self): - return self._pvt_ptr[0].reserved1 - @reserved1.setter - def reserved1(self, reserved1): - self._cyreserved1 = _HelperInputVoidPtr(reserved1) - self._pvt_ptr[0].reserved1 = self._cyreserved1.cptr - - @property def dstPitch(self): return self._pvt_ptr[0].dstPitch @@ -16498,10 +16376,6 @@ cdef class CUDA_MEMCPY_NODE_PARAMS_st: Must be zero - reserved : int - Must be zero - - copyCtx : CUcontext Context on which to run the node @@ -16542,12 +16416,6 @@ cdef class CUDA_MEMCPY_NODE_PARAMS_st: str_list += ['flags : '] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - - try: str_list += ['copyCtx : ' + str(self.copyCtx)] except ValueError: @@ -16571,14 +16439,6 @@ cdef class CUDA_MEMCPY_NODE_PARAMS_st: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, int reserved): - self._pvt_ptr[0].reserved = reserved - - @property def copyCtx(self): return self._copyCtx @@ -16948,10 +16808,6 @@ cdef class CUDA_ARRAY_SPARSE_PROPERTIES_st: CU_ARRAY_SPARSE_PROPERTIES_SINGLE_MIPTAIL - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -16998,12 +16854,6 @@ cdef class CUDA_ARRAY_SPARSE_PROPERTIES_st: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -17040,14 +16890,6 @@ cdef class CUDA_ARRAY_SPARSE_PROPERTIES_st: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class CUDA_ARRAY_MEMORY_REQUIREMENTS_st: """ CUDA array memory requirements @@ -17063,10 +16905,6 @@ cdef class CUDA_ARRAY_MEMORY_REQUIREMENTS_st: alignment requirement - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -17098,12 +16936,6 @@ cdef class CUDA_ARRAY_MEMORY_REQUIREMENTS_st: except ValueError: str_list += ['alignment : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -17124,14 +16956,6 @@ cdef class CUDA_ARRAY_MEMORY_REQUIREMENTS_st: self._pvt_ptr[0].alignment = alignment - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class anon_struct7: """ Attributes @@ -17504,13 +17328,6 @@ cdef class anon_struct10: cdef class anon_struct11: """ - Attributes - ---------- - - reserved : list[int] - - - Methods ------- getPtr() @@ -17529,23 +17346,10 @@ cdef class anon_struct11: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return self._pvt_ptr[0].res.reserved.reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].res.reserved.reserved = reserved - - cdef class anon_union4: """ Attributes @@ -17567,10 +17371,6 @@ cdef class anon_union4: - reserved : anon_struct11 - - - Methods ------- getPtr() @@ -17593,9 +17393,6 @@ cdef class anon_union4: self._pitch2D = anon_struct10(_ptr=self._pvt_ptr) - - self._reserved = anon_struct11(_ptr=self._pvt_ptr) - def __dealloc__(self): pass def getPtr(self): @@ -17627,12 +17424,6 @@ cdef class anon_union4: except ValueError: str_list += ['pitch2D : '] - - try: - str_list += ['reserved :\n' + '\n'.join([' ' + line for line in str(self.reserved).splitlines()])] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -17669,14 +17460,6 @@ cdef class anon_union4: string.memcpy(&self._pvt_ptr[0].res.pitch2D, pitch2D.getPtr(), sizeof(self._pvt_ptr[0].res.pitch2D)) - @property - def reserved(self): - return self._reserved - @reserved.setter - def reserved(self, reserved not None : anon_struct11): - string.memcpy(&self._pvt_ptr[0].res.reserved, reserved.getPtr(), sizeof(self._pvt_ptr[0].res.reserved)) - - cdef class CUDA_RESOURCE_DESC_st: """ CUDA Resource descriptor @@ -17809,10 +17592,6 @@ cdef class CUDA_TEXTURE_DESC_st: Border Color - reserved : list[int] - - - Methods ------- getPtr() @@ -17886,12 +17665,6 @@ cdef class CUDA_TEXTURE_DESC_st: except ValueError: str_list += ['borderColor : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -17968,14 +17741,6 @@ cdef class CUDA_TEXTURE_DESC_st: self._pvt_ptr[0].borderColor = borderColor - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class CUDA_RESOURCE_VIEW_DESC_st: """ Resource view descriptor @@ -18015,10 +17780,6 @@ cdef class CUDA_RESOURCE_VIEW_DESC_st: Last layer index - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -18086,12 +17847,6 @@ cdef class CUDA_RESOURCE_VIEW_DESC_st: except ValueError: str_list += ['lastLayer : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -18160,14 +17915,6 @@ cdef class CUDA_RESOURCE_VIEW_DESC_st: self._pvt_ptr[0].lastLayer = lastLayer - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class CUtensorMap_st: """ Tensor map descriptor. Requires compiler support for aligning to @@ -18690,10 +18437,6 @@ cdef class CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st: Flags must either be zero or CUDA_EXTERNAL_MEMORY_DEDICATED - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -18742,12 +18485,6 @@ cdef class CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -18784,14 +18521,6 @@ cdef class CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st: """ External memory buffer descriptor @@ -18811,10 +18540,6 @@ cdef class CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st: Flags reserved for future use. Must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -18852,12 +18577,6 @@ cdef class CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -18886,14 +18605,6 @@ cdef class CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st: """ External memory mipmap descriptor @@ -18914,10 +18625,6 @@ cdef class CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st: Total number of levels in the mipmap chain - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -18958,12 +18665,6 @@ cdef class CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st: except ValueError: str_list += ['numLevels : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -18992,14 +18693,6 @@ cdef class CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st: self._pvt_ptr[0].numLevels = numLevels - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class anon_struct13: """ Attributes @@ -19167,10 +18860,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st: Flags reserved for the future. Must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -19213,12 +18902,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -19247,14 +18930,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class anon_struct14: """ Attributes @@ -19308,10 +18983,6 @@ cdef class anon_union7: - reserved : unsigned long long - - - Methods ------- getPtr() @@ -19335,12 +19006,6 @@ cdef class anon_union7: except ValueError: str_list += ['fence : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -19354,14 +19019,6 @@ cdef class anon_union7: self._pvt_ptr[0].params.nvSciSync.fence = self._cyfence.cptr - @property - def reserved(self): - return self._pvt_ptr[0].params.nvSciSync.reserved - @reserved.setter - def reserved(self, unsigned long long reserved): - self._pvt_ptr[0].params.nvSciSync.reserved = reserved - - cdef class anon_struct15: """ Attributes @@ -19423,10 +19080,6 @@ cdef class anon_struct16: - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -19471,12 +19124,6 @@ cdef class anon_struct16: except ValueError: str_list += ['keyedMutex : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -19505,14 +19152,6 @@ cdef class anon_struct16: string.memcpy(&self._pvt_ptr[0].params.keyedMutex, keyedMutex.getPtr(), sizeof(self._pvt_ptr[0].params.keyedMutex)) - @property - def reserved(self): - return self._pvt_ptr[0].params.reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].params.reserved = reserved - - cdef class CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st: """ External semaphore signal parameters @@ -19535,10 +19174,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st: For all other types of CUexternalSemaphore, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -19573,12 +19208,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -19599,14 +19228,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class anon_struct17: """ Attributes @@ -19660,10 +19281,6 @@ cdef class anon_union8: - reserved : unsigned long long - - - Methods ------- getPtr() @@ -19687,12 +19304,6 @@ cdef class anon_union8: except ValueError: str_list += ['fence : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -19706,14 +19317,6 @@ cdef class anon_union8: self._pvt_ptr[0].params.nvSciSync.fence = self._cyfence.cptr - @property - def reserved(self): - return self._pvt_ptr[0].params.nvSciSync.reserved - @reserved.setter - def reserved(self, unsigned long long reserved): - self._pvt_ptr[0].params.nvSciSync.reserved = reserved - - cdef class anon_struct18: """ Attributes @@ -19793,10 +19396,6 @@ cdef class anon_struct19: - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -19841,12 +19440,6 @@ cdef class anon_struct19: except ValueError: str_list += ['keyedMutex : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -19875,14 +19468,6 @@ cdef class anon_struct19: string.memcpy(&self._pvt_ptr[0].params.keyedMutex, keyedMutex.getPtr(), sizeof(self._pvt_ptr[0].params.keyedMutex)) - @property - def reserved(self): - return self._pvt_ptr[0].params.reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].params.reserved = reserved - - cdef class CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st: """ External semaphore wait parameters @@ -19905,10 +19490,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st: For all other types of CUexternalSemaphore, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -19943,12 +19524,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -19969,14 +19544,6 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st: """ Semaphore signal node parameters @@ -20994,10 +20561,6 @@ cdef class CUarrayMapInfo_st: flags for future use, must be zero now. - reserved : list[unsigned int] - Reserved for future use, must be zero now. - - Methods ------- getPtr() @@ -21088,12 +20651,6 @@ cdef class CUarrayMapInfo_st: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -21178,14 +20735,6 @@ cdef class CUarrayMapInfo_st: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class CUmemLocation_st: """ Specifies a memory location. @@ -21273,10 +20822,6 @@ cdef class anon_struct22: - reserved : bytes - - - Methods ------- getPtr() @@ -21312,12 +20857,6 @@ cdef class anon_struct22: except ValueError: str_list += ['usage : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -21346,17 +20885,6 @@ cdef class anon_struct22: self._pvt_ptr[0].allocFlags.usage = usage - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].allocFlags.reserved, 4) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 4: - raise ValueError("reserved length must be 4, is " + str(len(reserved))) - for i, b in enumerate(reserved): - self._pvt_ptr[0].allocFlags.reserved[i] = b - - cdef class CUmemAllocationProp_st: """ Specifies the allocation properties for a allocation. @@ -21810,10 +21338,6 @@ cdef class CUmemPoolProps_st: Bitmask indicating intended usage for the pool. - reserved : bytes - reserved for future use, must be 0 - - Methods ------- getPtr() @@ -21872,12 +21396,6 @@ cdef class CUmemPoolProps_st: except ValueError: str_list += ['usage : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -21931,28 +21449,10 @@ cdef class CUmemPoolProps_st: self._pvt_ptr[0].usage = usage - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 54) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 54: - raise ValueError("reserved length must be 54, is " + str(len(reserved))) - for i, b in enumerate(reserved): - self._pvt_ptr[0].reserved[i] = b - - cdef class CUmemPoolPtrExportData_st: """ Opaque data for exporting a pool allocation - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -21973,26 +21473,10 @@ cdef class CUmemPoolPtrExportData_st: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 64) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 64: - raise ValueError("reserved length must be 64, is " + str(len(reserved))) - for i, b in enumerate(reserved): - self._pvt_ptr[0].reserved[i] = b - - cdef class CUmemcpyAttributes_st: """ Attributes specific to copies within a batch. For more details on @@ -23327,14 +22811,6 @@ cdef class CUgraphNodeParams_st: Type of the node - reserved0 : list[int] - Reserved. Must be zero. - - - reserved1 : list[long long] - Padding. Unused bytes must be zero. - - kernel : CUDA_KERNEL_NODE_PARAMS_v3 Kernel node parameters. @@ -23391,10 +22867,6 @@ cdef class CUgraphNodeParams_st: Padding as bytes - reserved2 : long long - Reserved bytes. Must be zero. - - Methods ------- getPtr() @@ -23462,18 +22934,6 @@ cdef class CUgraphNodeParams_st: str_list += ['type : '] - try: - str_list += ['reserved0 : ' + str(self.reserved0)] - except ValueError: - str_list += ['reserved0 : '] - - - try: - str_list += ['reserved1 : ' + str(self.reserved1)] - except ValueError: - str_list += ['reserved1 : '] - - try: str_list += ['kernel :\n' + '\n'.join([' ' + line for line in str(self.kernel).splitlines()])] except ValueError: @@ -23557,12 +23017,6 @@ cdef class CUgraphNodeParams_st: except ValueError: str_list += ['asBytes : '] - - try: - str_list += ['reserved2 : ' + str(self.reserved2)] - except ValueError: - str_list += ['reserved2 : '] - return '\n'.join(str_list) else: return '' @@ -23575,22 +23029,6 @@ cdef class CUgraphNodeParams_st: self._pvt_ptr[0].type = int(type) - @property - def reserved0(self): - return self._pvt_ptr[0].reserved0 - @reserved0.setter - def reserved0(self, reserved0): - self._pvt_ptr[0].reserved0 = reserved0 - - - @property - def reserved1(self): - return self._pvt_ptr[0].reserved1 - @reserved1.setter - def reserved1(self, reserved1): - self._pvt_ptr[0].reserved1 = reserved1 - - @property def kernel(self): return self._kernel @@ -23714,14 +23152,6 @@ cdef class CUgraphNodeParams_st: self._pvt_ptr[0].asBytes[i] = b - @property - def reserved2(self): - return self._pvt_ptr[0].reserved2 - @reserved2.setter - def reserved2(self, long long reserved2): - self._pvt_ptr[0].reserved2 = reserved2 - - cdef class CUcheckpointLockArgs_st: """ CUDA checkpoint optional lock arguments @@ -23734,14 +23164,6 @@ cdef class CUcheckpointLockArgs_st: no timeout - reserved0 : unsigned int - Reserved for future use, must be zero - - - reserved1 : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -23767,18 +23189,6 @@ cdef class CUcheckpointLockArgs_st: except ValueError: str_list += ['timeoutMs : '] - - try: - str_list += ['reserved0 : ' + str(self.reserved0)] - except ValueError: - str_list += ['reserved0 : '] - - - try: - str_list += ['reserved1 : ' + str(self.reserved1)] - except ValueError: - str_list += ['reserved1 : '] - return '\n'.join(str_list) else: return '' @@ -23791,34 +23201,10 @@ cdef class CUcheckpointLockArgs_st: self._pvt_ptr[0].timeoutMs = timeoutMs - @property - def reserved0(self): - return self._pvt_ptr[0].reserved0 - @reserved0.setter - def reserved0(self, unsigned int reserved0): - self._pvt_ptr[0].reserved0 = reserved0 - - - @property - def reserved1(self): - return [cuuint64_t(init_value=_reserved1) for _reserved1 in self._pvt_ptr[0].reserved1] - @reserved1.setter - def reserved1(self, reserved1): - self._pvt_ptr[0].reserved1 = reserved1 - - - cdef class CUcheckpointCheckpointArgs_st: """ CUDA checkpoint optional checkpoint arguments - Attributes - ---------- - - reserved : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -23839,24 +23225,10 @@ cdef class CUcheckpointCheckpointArgs_st: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return [cuuint64_t(init_value=_reserved) for _reserved in self._pvt_ptr[0].reserved] - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - - cdef class CUcheckpointGpuPair_st: """ CUDA checkpoint GPU UUID pairs for device remapping during restore @@ -23945,14 +23317,6 @@ cdef class CUcheckpointRestoreArgs_st: Number of gpu pairs to remap - reserved : bytes - Reserved for future use, must be zeroed - - - reserved : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -23989,12 +23353,6 @@ cdef class CUcheckpointRestoreArgs_st: except ValueError: str_list += ['gpuPairsCount : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -24031,45 +23389,10 @@ cdef class CUcheckpointRestoreArgs_st: self._pvt_ptr[0].gpuPairsCount = gpuPairsCount - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, {{struct_field_array_lengths['CUcheckpointRestoreArgs_st.reserved']}}) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != {{struct_field_array_lengths['CUcheckpointRestoreArgs_st.reserved']}}: - raise ValueError("reserved length must be {{struct_field_array_lengths['CUcheckpointRestoreArgs_st.reserved']}}, is " + str(len(reserved))) - if CHAR_MIN == 0: - for i, b in enumerate(reserved): - if b < 0 and b > -129: - b = b + 256 - self._pvt_ptr[0].reserved[i] = b - else: - for i, b in enumerate(reserved): - if b > 127 and b < 256: - b = b - 256 - self._pvt_ptr[0].reserved[i] = b - - - @property - def reserved(self): - return [cuuint64_t(init_value=_reserved) for _reserved in self._pvt_ptr[0].reserved] - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - - cdef class CUcheckpointUnlockArgs_st: """ CUDA checkpoint optional unlock arguments - Attributes - ---------- - - reserved : list[cuuint64_t] - Reserved for future use, must be zeroed - - Methods ------- getPtr() @@ -24090,24 +23413,10 @@ cdef class CUcheckpointUnlockArgs_st: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return [cuuint64_t(init_value=_reserved) for _reserved in self._pvt_ptr[0].reserved] - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - - cdef class CUmemDecompressParams_st: """ Structure describing the parameters that compose a single @@ -24149,10 +23458,6 @@ cdef class CUmemDecompressParams_st: The decompression algorithm to use. - padding : bytes - - - Methods ------- getPtr() @@ -24208,12 +23513,6 @@ cdef class CUmemDecompressParams_st: except ValueError: str_list += ['algo : '] - - try: - str_list += ['padding : ' + str(self.padding)] - except ValueError: - str_list += ['padding : '] - return '\n'.join(str_list) else: return '' @@ -24265,17 +23564,6 @@ cdef class CUmemDecompressParams_st: self._pvt_ptr[0].algo = int(algo) - @property - def padding(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].padding, 20) - @padding.setter - def padding(self, padding): - if len(padding) != 20: - raise ValueError("padding length must be 20, is " + str(len(padding))) - for i, b in enumerate(padding): - self._pvt_ptr[0].padding[i] = b - - cdef class CUlogicalEndpointFabricHandle_st: """ Fabric handle for a logical endpoint @@ -24777,13 +24065,6 @@ cdef class CUdevWorkqueueConfigResource_st: cdef class CUdevWorkqueueResource_st: """ - Attributes - ---------- - - reserved : bytes - Reserved for future use - - Methods ------- getPtr() @@ -24804,26 +24085,10 @@ cdef class CUdevWorkqueueResource_st: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 40) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 40: - raise ValueError("reserved length must be 40, is " + str(len(reserved))) - for i, b in enumerate(reserved): - self._pvt_ptr[0].reserved[i] = b - - cdef class CU_DEV_SM_RESOURCE_GROUP_PARAMS_st: """ Attributes @@ -24848,10 +24113,6 @@ cdef class CU_DEV_SM_RESOURCE_GROUP_PARAMS_st: CUdevSmResourceGroup_flags. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -24895,12 +24156,6 @@ cdef class CU_DEV_SM_RESOURCE_GROUP_PARAMS_st: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -24937,14 +24192,6 @@ cdef class CU_DEV_SM_RESOURCE_GROUP_PARAMS_st: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class CUdevResource_st: """ Attributes @@ -35463,7 +34710,7 @@ def cuMemSetAccess(ptr, size_t size, desc : Optional[tuple[CUmemAccessDesc] | li See Also -------- - :py:obj:`~.cuMemSetAccess`, :py:obj:`~.cuMemCreate`, :py:obj:`~.py`:obj:`~.cuMemMap` + :py:obj:`~.cuMemSetAccess`, :py:obj:`~.cuMemCreate`, :py:obj:`~.cuMemMap` """ desc = [] if desc is None else desc if not all(isinstance(_x, (CUmemAccessDesc,)) for _x in desc): @@ -36718,11 +35965,11 @@ def cuMulticastCreate(prop : Optional[CUmulticastObjectProp]): :py:obj:`~.cuMulticastBindAddr`, or :py:obj:`~.cuMulticastBindAddr_v2`. and can be unbound via :py:obj:`~.cuMulticastUnbind`. The total amount of memory that can be bound per device is specified by - :py:obj:`~.py`:obj:`~.CUmulticastObjectProp.size`. This size must be a - multiple of the value returned by :py:obj:`~.cuMulticastGetGranularity` - with the flag :py:obj:`~.CU_MULTICAST_GRANULARITY_MINIMUM`. For best - performance however, the size should be aligned to the value returned - by :py:obj:`~.cuMulticastGetGranularity` with the flag + :py:obj:`~.CUmulticastObjectProp.size`. This size must be a multiple of + the value returned by :py:obj:`~.cuMulticastGetGranularity` with the + flag :py:obj:`~.CU_MULTICAST_GRANULARITY_MINIMUM`. For best performance + however, the size should be aligned to the value returned by + :py:obj:`~.cuMulticastGetGranularity` with the flag :py:obj:`~.CU_MULTICAST_GRANULARITY_RECOMMENDED`. After all participating devices have been added, multicast objects can @@ -38081,13 +37328,12 @@ def cuPointerGetAttribute(attribute not None : CUpointer_attribute, ptr): :py:obj:`~.CUDA_POINTER_ATTRIBUTE_P2P_TOKENS`. - `ptr` must be a pointer to memory obtained from - :py:obj:`~.py`:obj:`~.cuMemAlloc()`. Note that p2pToken and - vaSpaceToken are only valid for the lifetime of the source - allocation. A subsequent allocation at the same address may return - completely different tokens. Querying this attribute has a side - effect of setting the attribute - :py:obj:`~.CU_POINTER_ATTRIBUTE_SYNC_MEMOPS` for the region of memory - that `ptr` points to. + :py:obj:`~.cuMemAlloc()`. Note that p2pToken and vaSpaceToken are + only valid for the lifetime of the source allocation. A subsequent + allocation at the same address may return completely different + tokens. Querying this attribute has a side effect of setting the + attribute :py:obj:`~.CU_POINTER_ATTRIBUTE_SYNC_MEMOPS` for the region + of memory that `ptr` points to. - :py:obj:`~.CU_POINTER_ATTRIBUTE_SYNC_MEMOPS`: diff --git a/cuda_bindings/cuda/bindings/nvfatbin.pyx b/cuda_bindings/cuda/bindings/nvfatbin.pyx index 309d2d751df..8b54e75e0f0 100644 --- a/cuda_bindings/cuda/bindings/nvfatbin.pyx +++ b/cuda_bindings/cuda/bindings/nvfatbin.pyx @@ -3,7 +3,7 @@ # SPDX-License-Identifier: Apache-2.0 # # This code was automatically generated across versions from 12.4.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=22dd0937e8e243f48b06a24f0c1819e09360d102541b621dfe1cdeaa55c2154c +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=2be5849c140c1ab6fc0408c1df7e885b2edb2a952aef35fd1c62f7ad5ce7fcb7 # <<<< PREAMBLE CONTENT >>>> @@ -117,7 +117,8 @@ cpdef intptr_t create(options, size_t options_count) except -1: """nvFatbinCreate creates a new handle. Args: - options (object): An array of strings, each containing a single option. It can be: + options (object): An array of strings, each containing a + single option. It can be: - an :class:`int` as the pointer address to the nested sequence, or - a Python sequence of :class:`int`\s, each of which is a pointer address @@ -147,8 +148,10 @@ cpdef add_ptx(intptr_t handle, code, size_t size, arch, identifier, options_cmd_ handle (intptr_t): nvFatbin handle. code (bytes): The PTX code. size (size_t): The size of the PTX code. - arch (str): The numerical architecture that this PTX is for (the XX of any sm_XX, lto_XX, or compute_XX). - identifier (str): Name of the PTX, useful when extracting the fatbin with tools like cuobjdump. + arch (str): The numerical architecture that this PTX is for + (the XX of any sm_XX, lto_XX, or compute_XX). + identifier (str): Name of the PTX, useful when extracting the + fatbin with tools like cuobjdump. options_cmd_line (str): Options used during JIT compilation. .. seealso:: `nvFatbinAddPTX` @@ -178,8 +181,10 @@ cpdef add_cubin(intptr_t handle, code, size_t size, arch, identifier): handle (intptr_t): nvFatbin handle. code (bytes): The cubin. size (size_t): The size of the cubin. - arch (str): The numerical architecture that this cubin is for (the XX of any sm_XX, lto_XX, or compute_XX). - identifier (str): Name of the cubin, useful when extracting the fatbin with tools like cuobjdump. + arch (str): The numerical architecture that this cubin is for + (the XX of any sm_XX, lto_XX, or compute_XX). + identifier (str): Name of the cubin, useful when extracting + the fatbin with tools like cuobjdump. .. seealso:: `nvFatbinAddCubin` """ @@ -204,8 +209,10 @@ cpdef add_ltoir(intptr_t handle, code, size_t size, arch, identifier, options_cm handle (intptr_t): nvFatbin handle. code (bytes): The LTOIR code. size (size_t): The size of the LTOIR code. - arch (str): The numerical architecture that this LTOIR is for (the XX of any sm_XX, lto_XX, or compute_XX). - identifier (str): Name of the LTOIR, useful when extracting the fatbin with tools like cuobjdump. + arch (str): The numerical architecture that this LTOIR is for + (the XX of any sm_XX, lto_XX, or compute_XX). + identifier (str): Name of the LTOIR, useful when extracting + the fatbin with tools like cuobjdump. options_cmd_line (str): Options used during JIT compilation. .. seealso:: `nvFatbinAddLTOIR` @@ -314,7 +321,8 @@ cpdef add_tile_ir(intptr_t handle, code, size_t size, identifier, options_cmd_li handle (intptr_t): nvFatbin handle. code (bytes): The Tile IR. size (size_t): The size of the Tile IR. - identifier (str): Name of the Tile IR, useful when extracting the fatbin with tools like cuobjdump. + identifier (str): Name of the Tile IR, useful when extracting + the fatbin with tools like cuobjdump. options_cmd_line (str): Options used during JIT compilation. .. seealso:: `nvFatbinAddTileIR` diff --git a/cuda_bindings/cuda/bindings/nvjitlink.pyx b/cuda_bindings/cuda/bindings/nvjitlink.pyx index eee6cc33923..866a8a4213d 100644 --- a/cuda_bindings/cuda/bindings/nvjitlink.pyx +++ b/cuda_bindings/cuda/bindings/nvjitlink.pyx @@ -3,7 +3,7 @@ # SPDX-License-Identifier: Apache-2.0 # # This code was automatically generated across versions from 12.0.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=85275f1596953f034c156776f8fe4f6e518dbb89ffedda994d8e78bfd9284246 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=73b6eb59cbe4fda520d37939d18d4625eb3818e37689796be45025a8aa877473 # <<<< PREAMBLE CONTENT >>>> @@ -117,7 +117,8 @@ cpdef intptr_t create(uint32_t num_options, options) except -1: Args: num_options (uint32_t): Number of options passed. - options (object): Array of size ``num_options`` of option strings. It can be: + options (object): Array of size ``num_options`` of option + strings. It can be: - an :class:`int` as the pointer address to the nested sequence, or - a Python sequence of :class:`int`\s, each of which is a pointer address diff --git a/cuda_bindings/cuda/bindings/nvml.pxd b/cuda_bindings/cuda/bindings/nvml.pxd index acc9900f069..f1ea7a144bc 100644 --- a/cuda_bindings/cuda/bindings/nvml.pxd +++ b/cuda_bindings/cuda/bindings/nvml.pxd @@ -4,7 +4,7 @@ # # This code was automatically generated across versions from 12.9.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=eb901f46ca6b6930935726541c32b3ea04f7f46b6090c4c2ad9cb62386c2028b +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=e1a348c4ffb12f72492093f32df3f186c11630337d891a567e92c266ecb80e88 from libc.stdint cimport intptr_t from .cynvml cimport * @@ -53,14 +53,10 @@ ctypedef nvmlMask255_t Mask255 ctypedef nvmlHostname_v1_t Hostname_v1 ctypedef nvmlUnrepairableMemoryStatus_v1_t UnrepairableMemoryStatus_v1 ctypedef nvmlRusdSettings_v1_t RusdSettings_v1 -ctypedef nvmlBBXTimeData_v1_t BBXTimeData_v1 -ctypedef nvmlRemappedRowsInfo_v2_t RemappedRowsInfo_v2 -ctypedef nvmlAccountingStats_v2_t AccountingStats_v2 ctypedef nvmlPowerValue_v2_t PowerValue_v2 ctypedef nvmlVgpuTypeMaxInstance_v1_t VgpuTypeMaxInstance_v1 ctypedef nvmlVgpuProcessUtilizationSample_t VgpuProcessUtilizationSample ctypedef nvmlGpuFabricInfo_t GpuFabricInfo -ctypedef nvmlCPERCursor_v1_t CPERCursor_v1 ctypedef nvmlSystemEventSetCreateRequest_v1_t SystemEventSetCreateRequest_v1 ctypedef nvmlSystemEventSetFreeRequest_v1_t SystemEventSetFreeRequest_v1 ctypedef nvmlSystemRegisterEventRequest_v1_t SystemRegisterEventRequest_v1 @@ -72,7 +68,6 @@ ctypedef nvmlWorkloadPowerProfileCurrentProfiles_v1_t WorkloadPowerProfileCurren ctypedef nvmlWorkloadPowerProfileRequestedProfiles_v1_t WorkloadPowerProfileRequestedProfiles_v1 ctypedef nvmlWorkloadPowerProfileUpdateProfiles_v1_t WorkloadPowerProfileUpdateProfiles_v1 ctypedef nvmlPRMTLV_v1_t PRMTLV_v1 -ctypedef nvmlGetCPER_v1_t GetCPER_v1 ctypedef nvmlVgpuSchedulerSetState_t VgpuSchedulerSetState ctypedef nvmlGpmMetricsGet_t GpmMetricsGet ctypedef nvmlPRMCounterList_v1_t PRMCounterList_v1 @@ -432,3 +427,7 @@ cpdef object device_get_vgpu_scheduler_log_v2(intptr_t device) cpdef object gpu_instance_get_vgpu_scheduler_log_v2(intptr_t gpu_instance) cpdef device_set_vgpu_scheduler_state_v2(intptr_t device, intptr_t p_scheduler_state) cpdef gpu_instance_set_vgpu_scheduler_state_v2(intptr_t gpu_instance, intptr_t p_scheduler_state) +cpdef object system_get_cper_v1() +cpdef object device_get_bbx_time_data_v1(intptr_t device) +cpdef object device_get_accounting_stats_v2(intptr_t device) +cpdef object device_get_remapped_rows_v2(intptr_t device) diff --git a/cuda_bindings/cuda/bindings/nvml.pyx b/cuda_bindings/cuda/bindings/nvml.pyx index a51d4264363..7e4b8877710 100644 --- a/cuda_bindings/cuda/bindings/nvml.pyx +++ b/cuda_bindings/cuda/bindings/nvml.pyx @@ -3,7 +3,7 @@ # SPDX-License-Identifier: Apache-2.0 # # This code was automatically generated across versions from 12.9.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=e47a16bd9956de14a991ded5d1aef667cdd26a141e27db5b2015b91be6918d3c +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=d1ffbac2395592e44a6f4cbdbdddac5ebeab85ab5557a5d9ca4efa822227ae38 # <<<< PREAMBLE CONTENT >>>> @@ -840,7 +840,7 @@ class GpmMetricId(_cyb_FastEnum): GPM_METRIC_HMMA_TENSOR_UTIL = (NVML_GPM_METRIC_HMMA_TENSOR_UTIL, "Percentage of time the GPU's SMs were doing HMMA tensor operations. 0.0 - 100.0.") GPM_METRIC_DMMA_TENSOR_UTIL = (NVML_GPM_METRIC_DMMA_TENSOR_UTIL, "Percentage of time the GPU's SMs were doing DMMA tensor operations. 0.0 - 100.0.") GPM_METRIC_IMMA_TENSOR_UTIL = (NVML_GPM_METRIC_IMMA_TENSOR_UTIL, "Percentage of time the GPU's SMs were doing IMMA tensor operations. 0.0 - 100.0.") - GPM_METRIC_DRAM_BW_UTIL = (NVML_GPM_METRIC_DRAM_BW_UTIL, 'Percentage of DRAM bw used vs theoretical maximum. 0.0 - 100.0 *\u200d/.') + GPM_METRIC_DRAM_BW_UTIL = (NVML_GPM_METRIC_DRAM_BW_UTIL, 'Percentage of DRAM bw used vs theoretical maximum. `0.0 - 100.0 */`.') GPM_METRIC_FP64_UTIL = (NVML_GPM_METRIC_FP64_UTIL, "Percentage of time the GPU's SMs were doing non-tensor FP64 math. 0.0 - 100.0.") GPM_METRIC_FP32_UTIL = (NVML_GPM_METRIC_FP32_UTIL, "Percentage of time the GPU's SMs were doing non-tensor FP32 math. 0.0 - 100.0.") GPM_METRIC_FP16_UTIL = (NVML_GPM_METRIC_FP16_UTIL, "Percentage of time the GPU's SMs were doing non-tensor FP16 math. 0.0 - 100.0.") @@ -16058,6 +16058,726 @@ cdef class VgpuSchedulerState_v2: return obj +cdef _get_bbx_time_data_v1_dtype_offsets(): + cdef nvmlBBXTimeData_v1_t pod + return _numpy.dtype({ + 'names': ['time_run'], + 'formats': [_numpy.uint32], + 'offsets': [ + (&(pod.timeRun)) - (&pod), + ], + 'itemsize': sizeof(nvmlBBXTimeData_v1_t), + }) + +bbx_time_data_v1_dtype = _get_bbx_time_data_v1_dtype_offsets() + +cdef class BBXTimeData_v1: + """Empty-initialize an instance of `nvmlBBXTimeData_v1_t`. + + + .. seealso:: `nvmlBBXTimeData_v1_t` + """ + cdef: + nvmlBBXTimeData_v1_t *_ptr + object _owner + bint _owned + bint _readonly + + def __init__(self): + self._ptr = _cyb_calloc(1, sizeof(nvmlBBXTimeData_v1_t)) + if self._ptr == NULL: + raise MemoryError("Error allocating BBXTimeData_v1") + self._owner = None + self._owned = True + self._readonly = False + + def __dealloc__(self): + cdef nvmlBBXTimeData_v1_t *ptr + if self._owned and self._ptr != NULL: + ptr = self._ptr + self._ptr = NULL + _cyb_free(ptr) + + def __repr__(self): + return f"<{__name__}.BBXTimeData_v1 object at {hex(id(self))}>" + + @property + def ptr(self): + """Get the pointer address to the data as Python :class:`int`.""" + return (self._ptr) + + cdef intptr_t _get_ptr(self): + return (self._ptr) + + def __int__(self): + return (self._ptr) + + def __eq__(self, other): + cdef BBXTimeData_v1 other_ + if not isinstance(other, BBXTimeData_v1): + return False + other_ = other + return (_cyb_memcmp((self._ptr), (other_._ptr), sizeof(nvmlBBXTimeData_v1_t)) == 0) + + def __getbuffer__(self, _cyb_cpython.Py_buffer *buffer, int flags): + _cyb___getbuffer(self, buffer, self._ptr, sizeof(nvmlBBXTimeData_v1_t), self._readonly) + + def __releasebuffer__(self, Py_buffer *buffer): + pass + + def __setitem__(self, key, val): + if key == 0 and isinstance(val, _numpy.ndarray): + self._ptr = _cyb_malloc(sizeof(nvmlBBXTimeData_v1_t)) + if self._ptr == NULL: + raise MemoryError("Error allocating BBXTimeData_v1") + _cyb_memcpy(self._ptr, val.ctypes.data, sizeof(nvmlBBXTimeData_v1_t)) + self._owner = None + self._owned = True + self._readonly = not val.flags.writeable + else: + setattr(self, key, val) + + @property + def time_run(self): + """int: [out] Cumulative number of seconds the GPU has had the driver loaded""" + return self._ptr[0].timeRun + + @time_run.setter + def time_run(self, val): + if self._readonly: + raise ValueError("This BBXTimeData_v1 instance is read-only") + self._ptr[0].timeRun = val + + @staticmethod + def from_buffer(buffer): + """Create an BBXTimeData_v1 instance with the memory from the given buffer.""" + return _cyb_from_buffer(buffer, sizeof(nvmlBBXTimeData_v1_t), BBXTimeData_v1) + + @staticmethod + def from_data(data): + """Create an BBXTimeData_v1 instance wrapping the given NumPy array. + + Args: + data (_numpy.ndarray): a single-element array of dtype `bbx_time_data_v1_dtype` holding the data. + """ + return _cyb_from_data(data, "bbx_time_data_v1_dtype", bbx_time_data_v1_dtype, BBXTimeData_v1) + + @staticmethod + def from_ptr(intptr_t ptr, bint readonly=False, object owner=None): + """Create an BBXTimeData_v1 instance wrapping the given pointer. + + Args: + ptr (intptr_t): pointer address as Python :class:`int` to the data. + owner (object): The Python object that owns the pointer. If not provided, data will be copied. + readonly (bool): whether the data is read-only (to the user). default is `False`. + """ + if ptr == 0: + raise ValueError("ptr must not be null (0)") + cdef BBXTimeData_v1 obj = BBXTimeData_v1.__new__(BBXTimeData_v1) + if owner is None: + obj._ptr = _cyb_malloc(sizeof(nvmlBBXTimeData_v1_t)) + if obj._ptr == NULL: + raise MemoryError("Error allocating BBXTimeData_v1") + _cyb_memcpy((obj._ptr), ptr, sizeof(nvmlBBXTimeData_v1_t)) + obj._owner = None + obj._owned = True + else: + obj._ptr = ptr + obj._owner = owner + obj._owned = False + obj._readonly = readonly + return obj + + +cdef _get_remapped_rows_info_v2_dtype_offsets(): + cdef nvmlRemappedRowsInfo_v2_t pod + return _numpy.dtype({ + 'names': ['corr_active_remaps', 'corr_inactive_remaps', 'unc_active_remaps', 'unc_inactive_remaps', 'b_pending', 'b_failure_occurred'], + 'formats': [_numpy.uint32, _numpy.uint32, _numpy.uint32, _numpy.uint32, _numpy.uint32, _numpy.uint32], + 'offsets': [ + (&(pod.corrActiveRemaps)) - (&pod), + (&(pod.corrInactiveRemaps)) - (&pod), + (&(pod.uncActiveRemaps)) - (&pod), + (&(pod.uncInactiveRemaps)) - (&pod), + (&(pod.bPending)) - (&pod), + (&(pod.bFailureOccurred)) - (&pod), + ], + 'itemsize': sizeof(nvmlRemappedRowsInfo_v2_t), + }) + +remapped_rows_info_v2_dtype = _get_remapped_rows_info_v2_dtype_offsets() + +cdef class RemappedRowsInfo_v2: + """Empty-initialize an instance of `nvmlRemappedRowsInfo_v2_t`. + + + .. seealso:: `nvmlRemappedRowsInfo_v2_t` + """ + cdef: + nvmlRemappedRowsInfo_v2_t *_ptr + object _owner + bint _owned + bint _readonly + + def __init__(self): + self._ptr = _cyb_calloc(1, sizeof(nvmlRemappedRowsInfo_v2_t)) + if self._ptr == NULL: + raise MemoryError("Error allocating RemappedRowsInfo_v2") + self._owner = None + self._owned = True + self._readonly = False + + def __dealloc__(self): + cdef nvmlRemappedRowsInfo_v2_t *ptr + if self._owned and self._ptr != NULL: + ptr = self._ptr + self._ptr = NULL + _cyb_free(ptr) + + def __repr__(self): + return f"<{__name__}.RemappedRowsInfo_v2 object at {hex(id(self))}>" + + @property + def ptr(self): + """Get the pointer address to the data as Python :class:`int`.""" + return (self._ptr) + + cdef intptr_t _get_ptr(self): + return (self._ptr) + + def __int__(self): + return (self._ptr) + + def __eq__(self, other): + cdef RemappedRowsInfo_v2 other_ + if not isinstance(other, RemappedRowsInfo_v2): + return False + other_ = other + return (_cyb_memcmp((self._ptr), (other_._ptr), sizeof(nvmlRemappedRowsInfo_v2_t)) == 0) + + def __getbuffer__(self, _cyb_cpython.Py_buffer *buffer, int flags): + _cyb___getbuffer(self, buffer, self._ptr, sizeof(nvmlRemappedRowsInfo_v2_t), self._readonly) + + def __releasebuffer__(self, Py_buffer *buffer): + pass + + def __setitem__(self, key, val): + if key == 0 and isinstance(val, _numpy.ndarray): + self._ptr = _cyb_malloc(sizeof(nvmlRemappedRowsInfo_v2_t)) + if self._ptr == NULL: + raise MemoryError("Error allocating RemappedRowsInfo_v2") + _cyb_memcpy(self._ptr, val.ctypes.data, sizeof(nvmlRemappedRowsInfo_v2_t)) + self._owner = None + self._owned = True + self._readonly = not val.flags.writeable + else: + setattr(self, key, val) + + @property + def corr_active_remaps(self): + """int: Number of active row remappings due to correctable errors.""" + return self._ptr[0].corrActiveRemaps + + @corr_active_remaps.setter + def corr_active_remaps(self, val): + if self._readonly: + raise ValueError("This RemappedRowsInfo_v2 instance is read-only") + self._ptr[0].corrActiveRemaps = val + + @property + def corr_inactive_remaps(self): + """int: Number of inactive row remappings due to correctable errors.""" + return self._ptr[0].corrInactiveRemaps + + @corr_inactive_remaps.setter + def corr_inactive_remaps(self, val): + if self._readonly: + raise ValueError("This RemappedRowsInfo_v2 instance is read-only") + self._ptr[0].corrInactiveRemaps = val + + @property + def unc_active_remaps(self): + """int: Number of active row remappings due to uncorrectable errors.""" + return self._ptr[0].uncActiveRemaps + + @unc_active_remaps.setter + def unc_active_remaps(self, val): + if self._readonly: + raise ValueError("This RemappedRowsInfo_v2 instance is read-only") + self._ptr[0].uncActiveRemaps = val + + @property + def unc_inactive_remaps(self): + """int: Number of inactive row remappings due to uncorrectable errors.""" + return self._ptr[0].uncInactiveRemaps + + @unc_inactive_remaps.setter + def unc_inactive_remaps(self, val): + if self._readonly: + raise ValueError("This RemappedRowsInfo_v2 instance is read-only") + self._ptr[0].uncInactiveRemaps = val + + @property + def b_pending(self): + """int: Whether or not there is any pending row remapping; 0 indicates not pending, 1 indicates pending.""" + return self._ptr[0].bPending + + @b_pending.setter + def b_pending(self, val): + if self._readonly: + raise ValueError("This RemappedRowsInfo_v2 instance is read-only") + self._ptr[0].bPending = val + + @property + def b_failure_occurred(self): + """int: Whether or not there's any row remapping failure in the past; 0 indicates no failure, 1 indicates failure occurred.""" + return self._ptr[0].bFailureOccurred + + @b_failure_occurred.setter + def b_failure_occurred(self, val): + if self._readonly: + raise ValueError("This RemappedRowsInfo_v2 instance is read-only") + self._ptr[0].bFailureOccurred = val + + @staticmethod + def from_buffer(buffer): + """Create an RemappedRowsInfo_v2 instance with the memory from the given buffer.""" + return _cyb_from_buffer(buffer, sizeof(nvmlRemappedRowsInfo_v2_t), RemappedRowsInfo_v2) + + @staticmethod + def from_data(data): + """Create an RemappedRowsInfo_v2 instance wrapping the given NumPy array. + + Args: + data (_numpy.ndarray): a single-element array of dtype `remapped_rows_info_v2_dtype` holding the data. + """ + return _cyb_from_data(data, "remapped_rows_info_v2_dtype", remapped_rows_info_v2_dtype, RemappedRowsInfo_v2) + + @staticmethod + def from_ptr(intptr_t ptr, bint readonly=False, object owner=None): + """Create an RemappedRowsInfo_v2 instance wrapping the given pointer. + + Args: + ptr (intptr_t): pointer address as Python :class:`int` to the data. + owner (object): The Python object that owns the pointer. If not provided, data will be copied. + readonly (bool): whether the data is read-only (to the user). default is `False`. + """ + if ptr == 0: + raise ValueError("ptr must not be null (0)") + cdef RemappedRowsInfo_v2 obj = RemappedRowsInfo_v2.__new__(RemappedRowsInfo_v2) + if owner is None: + obj._ptr = _cyb_malloc(sizeof(nvmlRemappedRowsInfo_v2_t)) + if obj._ptr == NULL: + raise MemoryError("Error allocating RemappedRowsInfo_v2") + _cyb_memcpy((obj._ptr), ptr, sizeof(nvmlRemappedRowsInfo_v2_t)) + obj._owner = None + obj._owned = True + else: + obj._ptr = ptr + obj._owner = owner + obj._owned = False + obj._readonly = readonly + return obj + + +cdef _get_accounting_stats_v2_dtype_offsets(): + cdef nvmlAccountingStats_v2_t pod + return _numpy.dtype({ + 'names': ['pid', 'is_running', 'gpu_utilization', 'memory_utilization', 'max_memory_usage', 'sample_count', 'sum_gpu_util', 'sum_fb_util', 'time', 'start_time'], + 'formats': [_numpy.uint32, _numpy.uint32, _numpy.uint32, _numpy.uint32, _numpy.uint64, _numpy.uint32, _numpy.uint64, _numpy.uint64, _numpy.uint64, _numpy.uint64], + 'offsets': [ + (&(pod.pid)) - (&pod), + (&(pod.isRunning)) - (&pod), + (&(pod.gpuUtilization)) - (&pod), + (&(pod.memoryUtilization)) - (&pod), + (&(pod.maxMemoryUsage)) - (&pod), + (&(pod.sampleCount)) - (&pod), + (&(pod.sumGpuUtil)) - (&pod), + (&(pod.sumFbUtil)) - (&pod), + (&(pod.time)) - (&pod), + (&(pod.startTime)) - (&pod), + ], + 'itemsize': sizeof(nvmlAccountingStats_v2_t), + }) + +accounting_stats_v2_dtype = _get_accounting_stats_v2_dtype_offsets() + +cdef class AccountingStats_v2: + """Empty-initialize an instance of `nvmlAccountingStats_v2_t`. + + + .. seealso:: `nvmlAccountingStats_v2_t` + """ + cdef: + nvmlAccountingStats_v2_t *_ptr + object _owner + bint _owned + bint _readonly + + def __init__(self): + self._ptr = _cyb_calloc(1, sizeof(nvmlAccountingStats_v2_t)) + if self._ptr == NULL: + raise MemoryError("Error allocating AccountingStats_v2") + self._owner = None + self._owned = True + self._readonly = False + + def __dealloc__(self): + cdef nvmlAccountingStats_v2_t *ptr + if self._owned and self._ptr != NULL: + ptr = self._ptr + self._ptr = NULL + _cyb_free(ptr) + + def __repr__(self): + return f"<{__name__}.AccountingStats_v2 object at {hex(id(self))}>" + + @property + def ptr(self): + """Get the pointer address to the data as Python :class:`int`.""" + return (self._ptr) + + cdef intptr_t _get_ptr(self): + return (self._ptr) + + def __int__(self): + return (self._ptr) + + def __eq__(self, other): + cdef AccountingStats_v2 other_ + if not isinstance(other, AccountingStats_v2): + return False + other_ = other + return (_cyb_memcmp((self._ptr), (other_._ptr), sizeof(nvmlAccountingStats_v2_t)) == 0) + + def __getbuffer__(self, _cyb_cpython.Py_buffer *buffer, int flags): + _cyb___getbuffer(self, buffer, self._ptr, sizeof(nvmlAccountingStats_v2_t), self._readonly) + + def __releasebuffer__(self, Py_buffer *buffer): + pass + + def __setitem__(self, key, val): + if key == 0 and isinstance(val, _numpy.ndarray): + self._ptr = _cyb_malloc(sizeof(nvmlAccountingStats_v2_t)) + if self._ptr == NULL: + raise MemoryError("Error allocating AccountingStats_v2") + _cyb_memcpy(self._ptr, val.ctypes.data, sizeof(nvmlAccountingStats_v2_t)) + self._owner = None + self._owned = True + self._readonly = not val.flags.writeable + else: + setattr(self, key, val) + + @property + def pid(self): + """int: Process Id of the target process to query stats for.""" + return self._ptr[0].pid + + @pid.setter + def pid(self, val): + if self._readonly: + raise ValueError("This AccountingStats_v2 instance is read-only") + self._ptr[0].pid = val + + @property + def is_running(self): + """int: Flag to represent if the process is running (1 for running, 0 for terminated).""" + return self._ptr[0].isRunning + + @is_running.setter + def is_running(self, val): + if self._readonly: + raise ValueError("This AccountingStats_v2 instance is read-only") + self._ptr[0].isRunning = val + + @property + def gpu_utilization(self): + """int: Percent of time over the process's lifetime during which one or more kernels was executing on the GPU. Utilization stats just like returned by nvmlDeviceGetUtilizationRates but for the life time of a process (not just the last sample period). Set to NVML_VALUE_NOT_AVAILABLE if nvmlDeviceGetUtilizationRates is not supported""" + return self._ptr[0].gpuUtilization + + @gpu_utilization.setter + def gpu_utilization(self, val): + if self._readonly: + raise ValueError("This AccountingStats_v2 instance is read-only") + self._ptr[0].gpuUtilization = val + + @property + def memory_utilization(self): + """int: Percent of time over the process's lifetime during which global (device) memory was being read or written. Set to NVML_VALUE_NOT_AVAILABLE if nvmlDeviceGetUtilizationRates is not supported""" + return self._ptr[0].memoryUtilization + + @memory_utilization.setter + def memory_utilization(self, val): + if self._readonly: + raise ValueError("This AccountingStats_v2 instance is read-only") + self._ptr[0].memoryUtilization = val + + @property + def max_memory_usage(self): + """int: Maximum total memory in bytes that was ever allocated by the process. Set to NVML_VALUE_NOT_AVAILABLE if nvmlProcessInfo_t->usedGpuMemory is not supported""" + return self._ptr[0].maxMemoryUsage + + @max_memory_usage.setter + def max_memory_usage(self, val): + if self._readonly: + raise ValueError("This AccountingStats_v2 instance is read-only") + self._ptr[0].maxMemoryUsage = val + + @property + def sample_count(self): + """int: The sample counts since the process starts.""" + return self._ptr[0].sampleCount + + @sample_count.setter + def sample_count(self, val): + if self._readonly: + raise ValueError("This AccountingStats_v2 instance is read-only") + self._ptr[0].sampleCount = val + + @property + def sum_gpu_util(self): + """int: The sum of process's GR engine utilization in unit of pct * 100.""" + return self._ptr[0].sumGpuUtil + + @sum_gpu_util.setter + def sum_gpu_util(self, val): + if self._readonly: + raise ValueError("This AccountingStats_v2 instance is read-only") + self._ptr[0].sumGpuUtil = val + + @property + def sum_fb_util(self): + """int: The sum of process's FB bandwidth utilization in unit of pct * 100.""" + return self._ptr[0].sumFbUtil + + @sum_fb_util.setter + def sum_fb_util(self, val): + if self._readonly: + raise ValueError("This AccountingStats_v2 instance is read-only") + self._ptr[0].sumFbUtil = val + + @property + def time(self): + """int: Amount of time in ms during which the compute context was active. The time is reported as 0 if the process is not terminated""" + return self._ptr[0].time + + @time.setter + def time(self, val): + if self._readonly: + raise ValueError("This AccountingStats_v2 instance is read-only") + self._ptr[0].time = val + + @property + def start_time(self): + """int: CPU Timestamp in usec representing start time for the process.""" + return self._ptr[0].startTime + + @start_time.setter + def start_time(self, val): + if self._readonly: + raise ValueError("This AccountingStats_v2 instance is read-only") + self._ptr[0].startTime = val + + @staticmethod + def from_buffer(buffer): + """Create an AccountingStats_v2 instance with the memory from the given buffer.""" + return _cyb_from_buffer(buffer, sizeof(nvmlAccountingStats_v2_t), AccountingStats_v2) + + @staticmethod + def from_data(data): + """Create an AccountingStats_v2 instance wrapping the given NumPy array. + + Args: + data (_numpy.ndarray): a single-element array of dtype `accounting_stats_v2_dtype` holding the data. + """ + return _cyb_from_data(data, "accounting_stats_v2_dtype", accounting_stats_v2_dtype, AccountingStats_v2) + + @staticmethod + def from_ptr(intptr_t ptr, bint readonly=False, object owner=None): + """Create an AccountingStats_v2 instance wrapping the given pointer. + + Args: + ptr (intptr_t): pointer address as Python :class:`int` to the data. + owner (object): The Python object that owns the pointer. If not provided, data will be copied. + readonly (bool): whether the data is read-only (to the user). default is `False`. + """ + if ptr == 0: + raise ValueError("ptr must not be null (0)") + cdef AccountingStats_v2 obj = AccountingStats_v2.__new__(AccountingStats_v2) + if owner is None: + obj._ptr = _cyb_malloc(sizeof(nvmlAccountingStats_v2_t)) + if obj._ptr == NULL: + raise MemoryError("Error allocating AccountingStats_v2") + _cyb_memcpy((obj._ptr), ptr, sizeof(nvmlAccountingStats_v2_t)) + obj._owner = None + obj._owned = True + else: + obj._ptr = ptr + obj._owner = owner + obj._owned = False + obj._readonly = readonly + return obj + + +cdef _get_cper_cursor_v1_dtype_offsets(): + cdef nvmlCPERCursor_v1_t pod + return _numpy.dtype({ + 'names': ['cper_type_mask', 'uuid', 'handle'], + 'formats': [_numpy.uint32, (_numpy.int8, 80), _numpy.uint64], + 'offsets': [ + (&(pod.cperTypeMask)) - (&pod), + (&(pod.uuid)) - (&pod), + (&(pod.handle)) - (&pod), + ], + 'itemsize': sizeof(nvmlCPERCursor_v1_t), + }) + +cper_cursor_v1_dtype = _get_cper_cursor_v1_dtype_offsets() + +cdef class CPERCursor_v1: + """Empty-initialize an instance of `nvmlCPERCursor_v1_t`. + + + .. seealso:: `nvmlCPERCursor_v1_t` + """ + cdef: + nvmlCPERCursor_v1_t *_ptr + object _owner + bint _owned + bint _readonly + + def __init__(self): + self._ptr = _cyb_calloc(1, sizeof(nvmlCPERCursor_v1_t)) + if self._ptr == NULL: + raise MemoryError("Error allocating CPERCursor_v1") + self._owner = None + self._owned = True + self._readonly = False + + def __dealloc__(self): + cdef nvmlCPERCursor_v1_t *ptr + if self._owned and self._ptr != NULL: + ptr = self._ptr + self._ptr = NULL + _cyb_free(ptr) + + def __repr__(self): + return f"<{__name__}.CPERCursor_v1 object at {hex(id(self))}>" + + @property + def ptr(self): + """Get the pointer address to the data as Python :class:`int`.""" + return (self._ptr) + + cdef intptr_t _get_ptr(self): + return (self._ptr) + + def __int__(self): + return (self._ptr) + + def __eq__(self, other): + cdef CPERCursor_v1 other_ + if not isinstance(other, CPERCursor_v1): + return False + other_ = other + return (_cyb_memcmp((self._ptr), (other_._ptr), sizeof(nvmlCPERCursor_v1_t)) == 0) + + def __getbuffer__(self, _cyb_cpython.Py_buffer *buffer, int flags): + _cyb___getbuffer(self, buffer, self._ptr, sizeof(nvmlCPERCursor_v1_t), self._readonly) + + def __releasebuffer__(self, Py_buffer *buffer): + pass + + def __setitem__(self, key, val): + if key == 0 and isinstance(val, _numpy.ndarray): + self._ptr = _cyb_malloc(sizeof(nvmlCPERCursor_v1_t)) + if self._ptr == NULL: + raise MemoryError("Error allocating CPERCursor_v1") + _cyb_memcpy(self._ptr, val.ctypes.data, sizeof(nvmlCPERCursor_v1_t)) + self._owner = None + self._owned = True + self._readonly = not val.flags.writeable + else: + setattr(self, key, val) + + @property + def cper_type_mask(self): + """int: [IN] Types of records to access. Bitmask of `nvmlCPERType_t` values. To change, reset `handle` to `NVML_CPER_CURSOR_HANDLE_INIT`.""" + return self._ptr[0].cperTypeMask + + @cper_type_mask.setter + def cper_type_mask(self, val): + if self._readonly: + raise ValueError("This CPERCursor_v1 instance is read-only") + self._ptr[0].cperTypeMask = val + + @property + def uuid(self): + """~_numpy.int8: (array of length 80).[IN] UUID of target to filter records for. Required for `NVML_CPER_ACCESS_TYPE_GPU`. To change, reset `handle` to `NVML_CPER_CURSOR_HANDLE_INIT`.""" + return _cyb_cpython.PyUnicode_FromString(self._ptr[0].uuid) + + @uuid.setter + def uuid(self, val): + if self._readonly: + raise ValueError("This CPERCursor_v1 instance is read-only") + cdef bytes buf = val.encode() + if len(buf) >= 80: + raise ValueError("String too long for field uuid, max length is 79") + cdef char *ptr = buf + _cyb_memcpy((self._ptr[0].uuid), ptr, 80) + + @property + def handle(self): + """int: [IN/OUT] Opaque handle tracking read position. Initialize to `NVML_CPER_CURSOR_HANDLE_INIT` on first call; pass the same ``nvmlCPERCursor_v1_t`` on the next call to continue. Caller must not interpret or modify.""" + return (self._ptr[0].handle) + + @handle.setter + def handle(self, val): + if self._readonly: + raise ValueError("This CPERCursor_v1 instance is read-only") + self._ptr[0].handle = val + + @staticmethod + def from_buffer(buffer): + """Create an CPERCursor_v1 instance with the memory from the given buffer.""" + return _cyb_from_buffer(buffer, sizeof(nvmlCPERCursor_v1_t), CPERCursor_v1) + + @staticmethod + def from_data(data): + """Create an CPERCursor_v1 instance wrapping the given NumPy array. + + Args: + data (_numpy.ndarray): a single-element array of dtype `cper_cursor_v1_dtype` holding the data. + """ + return _cyb_from_data(data, "cper_cursor_v1_dtype", cper_cursor_v1_dtype, CPERCursor_v1) + + @staticmethod + def from_ptr(intptr_t ptr, bint readonly=False, object owner=None): + """Create an CPERCursor_v1 instance wrapping the given pointer. + + Args: + ptr (intptr_t): pointer address as Python :class:`int` to the data. + owner (object): The Python object that owns the pointer. If not provided, data will be copied. + readonly (bool): whether the data is read-only (to the user). default is `False`. + """ + if ptr == 0: + raise ValueError("ptr must not be null (0)") + cdef CPERCursor_v1 obj = CPERCursor_v1.__new__(CPERCursor_v1) + if owner is None: + obj._ptr = _cyb_malloc(sizeof(nvmlCPERCursor_v1_t)) + if obj._ptr == NULL: + raise MemoryError("Error allocating CPERCursor_v1") + _cyb_memcpy((obj._ptr), ptr, sizeof(nvmlCPERCursor_v1_t)) + obj._owner = None + obj._owned = True + else: + obj._ptr = ptr + obj._owner = owner + obj._owned = False + obj._readonly = readonly + return obj + + cdef _get_excluded_device_info_dtype_offsets(): cdef nvmlExcludedDeviceInfo_t pod return _numpy.dtype({ @@ -20030,6 +20750,162 @@ cdef class VgpuSchedulerLogInfo_v2: return obj +cdef _get_get_cper_v1_dtype_offsets(): + cdef nvmlGetCPER_v1_t pod + return _numpy.dtype({ + 'names': ['cursor', 'buffer', 'buffer_size'], + 'formats': [cper_cursor_v1_dtype, _numpy.intp, _numpy.uint32], + 'offsets': [ + (&(pod.cursor)) - (&pod), + (&(pod.buffer)) - (&pod), + (&(pod.bufferSize)) - (&pod), + ], + 'itemsize': sizeof(nvmlGetCPER_v1_t), + }) + +get_cper_v1_dtype = _get_get_cper_v1_dtype_offsets() + +cdef class GetCPER_v1: + """Empty-initialize an instance of `nvmlGetCPER_v1_t`. + + + .. seealso:: `nvmlGetCPER_v1_t` + """ + cdef: + nvmlGetCPER_v1_t *_ptr + object _owner + bint _owned + bint _readonly + + def __init__(self): + self._ptr = _cyb_calloc(1, sizeof(nvmlGetCPER_v1_t)) + if self._ptr == NULL: + raise MemoryError("Error allocating GetCPER_v1") + self._owner = None + self._owned = True + self._readonly = False + + def __dealloc__(self): + cdef nvmlGetCPER_v1_t *ptr + if self._owned and self._ptr != NULL: + ptr = self._ptr + self._ptr = NULL + _cyb_free(ptr) + + def __repr__(self): + return f"<{__name__}.GetCPER_v1 object at {hex(id(self))}>" + + @property + def ptr(self): + """Get the pointer address to the data as Python :class:`int`.""" + return (self._ptr) + + cdef intptr_t _get_ptr(self): + return (self._ptr) + + def __int__(self): + return (self._ptr) + + def __eq__(self, other): + cdef GetCPER_v1 other_ + if not isinstance(other, GetCPER_v1): + return False + other_ = other + return (_cyb_memcmp((self._ptr), (other_._ptr), sizeof(nvmlGetCPER_v1_t)) == 0) + + def __getbuffer__(self, _cyb_cpython.Py_buffer *buffer, int flags): + _cyb___getbuffer(self, buffer, self._ptr, sizeof(nvmlGetCPER_v1_t), self._readonly) + + def __releasebuffer__(self, Py_buffer *buffer): + pass + + def __setitem__(self, key, val): + if key == 0 and isinstance(val, _numpy.ndarray): + self._ptr = _cyb_malloc(sizeof(nvmlGetCPER_v1_t)) + if self._ptr == NULL: + raise MemoryError("Error allocating GetCPER_v1") + _cyb_memcpy(self._ptr, val.ctypes.data, sizeof(nvmlGetCPER_v1_t)) + self._owner = None + self._owned = True + self._readonly = not val.flags.writeable + else: + setattr(self, key, val) + + @property + def cursor(self): + """CPERCursor_v1: [IN/OUT] Query parameters and cursor. See `nvmlCPERCursor_v1_t`""" + return CPERCursor_v1.from_ptr(&(self._ptr[0].cursor), self._readonly, self) + + @cursor.setter + def cursor(self, val): + if self._readonly: + raise ValueError("This GetCPER_v1 instance is read-only") + cdef CPERCursor_v1 val_ = val + _cyb_memcpy(&(self._ptr[0].cursor), (val_._get_ptr()), sizeof(nvmlCPERCursor_v1_t) * 1) + + @property + def buffer(self): + """str: [OUT] Buffer to be filled (allocated by client). May be NULL for size query.""" + return (self._ptr[0].buffer) + + @buffer.setter + def buffer(self, val): + if self._readonly: + raise ValueError("This GetCPER_v1 instance is read-only") + self._ptr[0].buffer = val + + @property + def buffer_size(self): + """int: [IN/OUT] Size of `buffer`. Set to 0 with `buffer` NULL to query required size. On return, set to required or used size; 0 means no (more) records.""" + return self._ptr[0].bufferSize + + @buffer_size.setter + def buffer_size(self, val): + if self._readonly: + raise ValueError("This GetCPER_v1 instance is read-only") + self._ptr[0].bufferSize = val + + @staticmethod + def from_buffer(buffer): + """Create an GetCPER_v1 instance with the memory from the given buffer.""" + return _cyb_from_buffer(buffer, sizeof(nvmlGetCPER_v1_t), GetCPER_v1) + + @staticmethod + def from_data(data): + """Create an GetCPER_v1 instance wrapping the given NumPy array. + + Args: + data (_numpy.ndarray): a single-element array of dtype `get_cper_v1_dtype` holding the data. + """ + return _cyb_from_data(data, "get_cper_v1_dtype", get_cper_v1_dtype, GetCPER_v1) + + @staticmethod + def from_ptr(intptr_t ptr, bint readonly=False, object owner=None): + """Create an GetCPER_v1 instance wrapping the given pointer. + + Args: + ptr (intptr_t): pointer address as Python :class:`int` to the data. + owner (object): The Python object that owns the pointer. If not provided, data will be copied. + readonly (bool): whether the data is read-only (to the user). default is `False`. + """ + if ptr == 0: + raise ValueError("ptr must not be null (0)") + cdef GetCPER_v1 obj = GetCPER_v1.__new__(GetCPER_v1) + if owner is None: + obj._ptr = _cyb_malloc(sizeof(nvmlGetCPER_v1_t)) + if obj._ptr == NULL: + raise MemoryError("Error allocating GetCPER_v1") + _cyb_memcpy((obj._ptr), ptr, sizeof(nvmlGetCPER_v1_t)) + obj._owner = None + obj._owned = True + else: + obj._ptr = ptr + obj._owner = owner + obj._owned = False + obj._readonly = readonly + return obj + + cdef _get_vgpu_instances_utilization_info_v1_dtype_offsets(): cdef nvmlVgpuInstancesUtilizationInfo_v1_t pod return _numpy.dtype({ @@ -21747,7 +22623,8 @@ cpdef unsigned int unit_get_count() except? 0: """Retrieves the number of units in the system. Returns: - unsigned int: Reference in which to return the number of units. + unsigned int: Reference in which to return the number of + units. .. seealso:: `nvmlUnitGetCount` """ @@ -21762,7 +22639,8 @@ cpdef intptr_t unit_get_handle_by_index(unsigned int index) except? 0: """Acquire the handle for a particular unit, based on its index. Args: - index (unsigned int): The index of the target unit, >= 0 and < ``unitCount``. + index (unsigned int): The index of the target unit, >= 0 and < + ``unitCount``. Returns: intptr_t: Reference in which to return the unit handle. @@ -21783,7 +22661,8 @@ cpdef object unit_get_unit_info(intptr_t unit): unit (intptr_t): The identifier of the target unit. Returns: - nvmlUnitInfo_t: Reference in which to return the unit information. + nvmlUnitInfo_t: Reference in which to return the unit + information. .. seealso:: `nvmlUnitGetUnitInfo` """ @@ -21802,7 +22681,8 @@ cpdef object unit_get_led_state(intptr_t unit): unit (intptr_t): The identifier of the target unit. Returns: - nvmlLedState_t: Reference in which to return the current LED state. + nvmlLedState_t: Reference in which to return the current LED + state. .. seealso:: `nvmlUnitGetLedState` """ @@ -21821,7 +22701,8 @@ cpdef object unit_get_psu_info(intptr_t unit): unit (intptr_t): The identifier of the target unit. Returns: - nvmlPSUInfo_t: Reference in which to return the PSU information. + nvmlPSUInfo_t: Reference in which to return the PSU + information. .. seealso:: `nvmlUnitGetPsuInfo` """ @@ -21841,7 +22722,8 @@ cpdef unsigned int unit_get_temperature(intptr_t unit, unsigned int type) except type (unsigned int): The type of reading to take. Returns: - unsigned int: Reference in which to return the intake temperature. + unsigned int: Reference in which to return the intake + temperature. .. seealso:: `nvmlUnitGetTemperature` """ @@ -21859,7 +22741,8 @@ cpdef object unit_get_fan_speed_info(intptr_t unit): unit (intptr_t): The identifier of the target unit. Returns: - nvmlUnitFanSpeeds_t: Reference in which to return the fan speed information. + nvmlUnitFanSpeeds_t: Reference in which to return the fan + speed information. .. seealso:: `nvmlUnitGetFanSpeedInfo` """ @@ -21875,7 +22758,8 @@ cpdef unsigned int device_get_count_v2() except? 0: """Retrieves the number of compute devices in the system. A compute device is a single GPU. Returns: - unsigned int: Reference in which to return the number of accessible devices. + unsigned int: Reference in which to return the number of + accessible devices. .. seealso:: `nvmlDeviceGetCount_v2` """ @@ -21909,7 +22793,8 @@ cpdef intptr_t device_get_handle_by_index_v2(unsigned int index) except? 0: """Acquire the handle for a particular device, based on its index. Args: - index (unsigned int): The index of the target GPU, >= 0 and < ``accessibleDevices``. + index (unsigned int): The index of the target GPU, >= 0 and < + ``accessibleDevices``. Returns: intptr_t: Reference in which to return the device handle. @@ -21952,7 +22837,8 @@ cpdef intptr_t device_get_handle_by_uuid(uuid) except? 0: uuid (str): The UUID of the target GPU or MIG instance. Returns: - intptr_t: Reference in which to return the device handle or MIG device handle. + intptr_t: Reference in which to return the device handle or + MIG device handle. .. seealso:: `nvmlDeviceGetHandleByUUID` """ @@ -21971,7 +22857,11 @@ cpdef intptr_t device_get_handle_by_pci_bus_id_v2(pci_bus_id) except? 0: """Acquire the handle for a particular device, based on its PCI bus id. Args: - pci_bus_id (str): The PCI bus id of the target GPU Accept the following formats (all numbers in hexadecimal): domain:bus:device.function in format x:x:x.x domain:bus:device in format x:x:x bus:device.function in format x:x.x. + pci_bus_id (str): The PCI bus id of the target GPU Accept the + following formats (all numbers in hexadecimal): + domain:bus:device.function in format x:x:x.x + domain:bus:device in format x:x:x bus:device.function in + format x:x.x. Returns: intptr_t: Reference in which to return the device handle. @@ -22033,7 +22923,8 @@ cpdef unsigned int device_get_index(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the NVML index of the device. + unsigned int: Reference in which to return the NVML index of + the device. .. seealso:: `nvmlDeviceGetIndex` """ @@ -22051,7 +22942,8 @@ cpdef str device_get_serial(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - char: Reference in which to return the board/module serial number. + char: Reference in which to return the board/module serial + number. .. seealso:: `nvmlDeviceGetSerial` """ @@ -22088,7 +22980,8 @@ cpdef object device_get_c2c_mode_info_v(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlC2cModeInfo_v1_t: Output struct containing the device's C2C Mode info. + nvmlC2cModeInfo_v1_t: Output struct containing the device's + C2C Mode info. .. seealso:: `nvmlDeviceGetC2cModeInfoV` """ @@ -22105,11 +22998,14 @@ cpdef object device_get_memory_affinity(intptr_t device, unsigned int node_set_s Args: device (intptr_t): The identifier of the target device. - node_set_size (unsigned int): The size of the node_set array that is safe to access. + node_set_size (unsigned int): The size of the node_set array + that is safe to access. scope (unsigned int): Scope that change the default behavior. Returns: - unsigned long: Array reference in which to return a bitmask of NODEs, 64 NODEs per unsigned long on 64-bit machines, 32 on 32-bit machines. + unsigned long: Array reference in which to return a bitmask of + NODEs, 64 NODEs per unsigned long on 64-bit machines, 32 + on 32-bit machines. .. seealso:: `nvmlDeviceGetMemoryAffinity` """ @@ -22128,11 +23024,14 @@ cpdef object device_get_cpu_affinity_within_scope(intptr_t device, unsigned int Args: device (intptr_t): The identifier of the target device. - cpu_set_size (unsigned int): The size of the cpu_set array that is safe to access. + cpu_set_size (unsigned int): The size of the cpu_set array + that is safe to access. scope (unsigned int): Scope that change the default behavior. Returns: - unsigned long: Array reference in which to return a bitmask of CPUs, 64 CPUs per unsigned long on 64-bit machines, 32 on 32-bit machines. + unsigned long: Array reference in which to return a bitmask of + CPUs, 64 CPUs per unsigned long on 64-bit machines, 32 on + 32-bit machines. .. seealso:: `nvmlDeviceGetCpuAffinityWithinScope` """ @@ -22151,10 +23050,13 @@ cpdef object device_get_cpu_affinity(intptr_t device, unsigned int cpu_set_size) Args: device (intptr_t): The identifier of the target device. - cpu_set_size (unsigned int): The size of the cpu_set array that is safe to access. + cpu_set_size (unsigned int): The size of the cpu_set array + that is safe to access. Returns: - unsigned long: Array reference in which to return a bitmask of CPUs, 64 CPUs per unsigned long on 64-bit machines, 32 on 32-bit machines. + unsigned long: Array reference in which to return a bitmask of + CPUs, 64 CPUs per unsigned long on 64-bit machines, 32 on + 32-bit machines. .. seealso:: `nvmlDeviceGetCpuAffinity` """ @@ -22237,10 +23139,12 @@ cpdef int device_get_p2p_status(intptr_t device1, intptr_t device2, int p2p_inde Args: device1 (intptr_t): The first device. device2 (intptr_t): The second device. - p2p_index (GpuP2PCapsIndex): p2p Capability Index being looked for between ``device1`` and ``device2``. + p2p_index (GpuP2PCapsIndex): p2p Capability Index being looked + for between ``device1`` and ``device2``. Returns: - int: Reference in which to return the status of the ``p2p_index`` between ``device1`` and ``device2``. + int: Reference in which to return the status of the + ``p2p_index`` between ``device1`` and ``device2``. .. seealso:: `nvmlDeviceGetP2PStatus` """ @@ -22277,7 +23181,8 @@ cpdef unsigned int device_get_minor_number(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the minor number for the device. + unsigned int: Reference in which to return the minor number + for the device. .. seealso:: `nvmlDeviceGetMinorNumber` """ @@ -22353,7 +23258,8 @@ cpdef unsigned int device_get_inforom_configuration_checksum(intptr_t device) ex device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the infoROM configuration checksum. + unsigned int: Reference in which to return the infoROM + configuration checksum. .. seealso:: `nvmlDeviceGetInforomConfigurationChecksum` """ @@ -22442,7 +23348,8 @@ cpdef int device_get_persistence_mode(intptr_t device) except? -1: device (intptr_t): The identifier of the target device. Returns: - int: Reference in which to return the current driver persistence mode. + int: Reference in which to return the current driver + persistence mode. .. seealso:: `nvmlDeviceGetPersistenceMode` """ @@ -22460,7 +23367,8 @@ cpdef object device_get_pci_info_ext(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlPciInfoExt_v1_t: Reference in which to return the PCI info. + nvmlPciInfoExt_v1_t: Reference in which to return the PCI + info. .. seealso:: `nvmlDeviceGetPciInfoExt` """ @@ -22499,7 +23407,8 @@ cpdef unsigned int device_get_max_pcie_link_generation(intptr_t device) except? device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the max PCIe link generation. + unsigned int: Reference in which to return the max PCIe link + generation. .. seealso:: `nvmlDeviceGetMaxPcieLinkGeneration` """ @@ -22517,7 +23426,8 @@ cpdef unsigned int device_get_gpu_max_pcie_link_generation(intptr_t device) exce device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the max PCIe link generation. + unsigned int: Reference in which to return the max PCIe link + generation. .. seealso:: `nvmlDeviceGetGpuMaxPcieLinkGeneration` """ @@ -22535,7 +23445,8 @@ cpdef unsigned int device_get_max_pcie_link_width(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the max PCIe link generation. + unsigned int: Reference in which to return the max PCIe link + generation. .. seealso:: `nvmlDeviceGetMaxPcieLinkWidth` """ @@ -22553,7 +23464,8 @@ cpdef unsigned int device_get_curr_pcie_link_generation(intptr_t device) except? device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the current PCIe link generation. + unsigned int: Reference in which to return the current PCIe + link generation. .. seealso:: `nvmlDeviceGetCurrPcieLinkGeneration` """ @@ -22571,7 +23483,8 @@ cpdef unsigned int device_get_curr_pcie_link_width(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the current PCIe link generation. + unsigned int: Reference in which to return the current PCIe + link generation. .. seealso:: `nvmlDeviceGetCurrPcieLinkWidth` """ @@ -22587,7 +23500,8 @@ cpdef unsigned int device_get_pcie_throughput(intptr_t device, int counter) exce Args: device (intptr_t): The identifier of the target device. - counter (PcieUtilCounter): The specific counter that should be queried ``nvmlPcieUtilCounter_t``. + counter (PcieUtilCounter): The specific counter that should be + queried ``nvmlPcieUtilCounter_t``. Returns: unsigned int: Reference in which to return throughput in KB/s. @@ -22608,7 +23522,8 @@ cpdef unsigned int device_get_pcie_replay_counter(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the counter's value. + unsigned int: Reference in which to return the counter's + value. .. seealso:: `nvmlDeviceGetPcieReplayCounter` """ @@ -22627,7 +23542,8 @@ cpdef unsigned int device_get_clock_info(intptr_t device, int type) except? 0: type (ClockType): Identify which clock domain to query. Returns: - unsigned int: Reference in which to return the clock speed in MHz. + unsigned int: Reference in which to return the clock speed in + MHz. .. seealso:: `nvmlDeviceGetClockInfo` """ @@ -22646,7 +23562,8 @@ cpdef unsigned int device_get_max_clock_info(intptr_t device, int type) except? type (ClockType): Identify which clock domain to query. Returns: - unsigned int: Reference in which to return the clock speed in MHz. + unsigned int: Reference in which to return the clock speed in + MHz. .. seealso:: `nvmlDeviceGetMaxClockInfo` """ @@ -22681,7 +23598,8 @@ cpdef unsigned int device_get_clock(intptr_t device, int clock_type, int clock_i Args: device (intptr_t): The identifier of the target device. clock_type (ClockType): Identify which clock domain to query. - clock_id (ClockId): Identify which clock in the domain to query. + clock_id (ClockId): Identify which clock in the domain to + query. Returns: unsigned int: Reference in which to return the clock in MHz. @@ -22744,7 +23662,8 @@ cpdef object device_get_supported_graphics_clocks(intptr_t device, unsigned int Args: device (intptr_t): The identifier of the target device. - memory_clock_m_hz (unsigned int): Memory clock for which to return possible graphics clocks. + memory_clock_m_hz (unsigned int): Memory clock for which to + return possible graphics clocks. Returns: unsigned int: Reference in which to return the clocks in MHz. @@ -22774,8 +23693,11 @@ cpdef tuple device_get_auto_boosted_clocks_enabled(intptr_t device): Returns: A 2-tuple containing: - - int: Where to store the current state of Auto Boosted clocks of the target device. - - int: Where to store the default Auto Boosted clocks behavior of the target device that the device will revert to when no applications are using the GPU. + - int: Where to store the current state of Auto Boosted clocks + of the target device. + - int: Where to store the default Auto Boosted clocks behavior + of the target device that the device will revert to when + no applications are using the GPU. .. seealso:: `nvmlDeviceGetAutoBoostedClocksEnabled` """ @@ -22794,7 +23716,8 @@ cpdef unsigned int device_get_fan_speed(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the fan speed percentage. + unsigned int: Reference in which to return the fan speed + percentage. .. seealso:: `nvmlDeviceGetFanSpeed` """ @@ -22813,7 +23736,8 @@ cpdef unsigned int device_get_fan_speed_v2(intptr_t device, unsigned int fan) ex fan (unsigned int): The index of the target fan, zero indexed. Returns: - unsigned int: Reference in which to return the fan speed percentage. + unsigned int: Reference in which to return the fan speed + percentage. .. seealso:: `nvmlDeviceGetFanSpeed_v2` """ @@ -22832,7 +23756,8 @@ cpdef unsigned int device_get_target_fan_speed(intptr_t device, unsigned int fan fan (unsigned int): The index of the target fan, zero indexed. Returns: - unsigned int: Reference in which to return the fan speed percentage. + unsigned int: Reference in which to return the fan speed + percentage. .. seealso:: `nvmlDeviceGetTargetFanSpeed` """ @@ -22873,7 +23798,8 @@ cpdef unsigned int device_get_fan_control_policy_v2(intptr_t device, unsigned in fan (unsigned int): The index of the target fan, zero indexed. Returns: - unsigned int: Reference in which to return the fan control ``policy``. + unsigned int: Reference in which to return the fan control + ``policy``. .. seealso:: `nvmlDeviceGetFanControlPolicy_v2` """ @@ -22909,7 +23835,9 @@ cpdef object device_get_cooler_info(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlCoolerInfo_v1_t: Structure specifying the cooler's control signal characteristics (out) and the target that cooler cools (out). + nvmlCoolerInfo_v1_t: Structure specifying the cooler's control + signal characteristics (out) and the target that cooler + cools (out). .. seealso:: `nvmlDeviceGetCoolerInfo` """ @@ -22927,10 +23855,12 @@ cpdef unsigned int device_get_temperature_threshold(intptr_t device, int thresho Args: device (intptr_t): The identifier of the target device. - threshold_type (TemperatureThresholds): The type of threshold value queried. + threshold_type (TemperatureThresholds): The type of threshold + value queried. Returns: - unsigned int: Reference in which to return the temperature reading. + unsigned int: Reference in which to return the temperature + reading. .. seealso:: `nvmlDeviceGetTemperatureThreshold` """ @@ -22949,7 +23879,8 @@ cpdef object device_get_thermal_settings(intptr_t device, unsigned int sensor_in sensor_index (unsigned int): The index of the thermal sensor. Returns: - nvmlGpuThermalSettings_t: Reference in which to return the thermal sensor information. + nvmlGpuThermalSettings_t: Reference in which to return the + thermal sensor information. .. seealso:: `nvmlDeviceGetThermalSettings` """ @@ -22968,7 +23899,8 @@ cpdef int device_get_performance_state(intptr_t device) except? -1: device (intptr_t): The identifier of the target device. Returns: - int: Reference in which to return the performance state reading. + int: Reference in which to return the performance state + reading. .. seealso:: `nvmlDeviceGetPerformanceState` """ @@ -22986,7 +23918,8 @@ cpdef unsigned long long device_get_current_clocks_event_reasons(intptr_t device device (intptr_t): The identifier of the target device. Returns: - unsigned long long: Reference in which to return bitmask of active clocks event reasons. + unsigned long long: Reference in which to return bitmask of + active clocks event reasons. .. seealso:: `nvmlDeviceGetCurrentClocksEventReasons` """ @@ -23004,7 +23937,8 @@ cpdef unsigned long long device_get_supported_clocks_event_reasons(intptr_t devi device (intptr_t): The identifier of the target device. Returns: - unsigned long long: Reference in which to return bitmask of supported clocks event reasons. + unsigned long long: Reference in which to return bitmask of + supported clocks event reasons. .. seealso:: `nvmlDeviceGetSupportedClocksEventReasons` """ @@ -23022,7 +23956,8 @@ cpdef int device_get_power_state(intptr_t device) except? -1: device (intptr_t): The identifier of the target device. Returns: - int: Reference in which to return the performance state reading. + int: Reference in which to return the performance state + reading. .. seealso:: `nvmlDeviceGetPowerState` """ @@ -23081,8 +24016,10 @@ cpdef tuple device_get_min_max_clock_of_p_state(intptr_t device, int type, int p Returns: A 2-tuple containing: - - unsigned int: Reference in which to return min clock frequency. - - unsigned int: Reference in which to return max clock frequency. + - unsigned int: Reference in which to return min clock + frequency. + - unsigned int: Reference in which to return max clock + frequency. .. seealso:: `nvmlDeviceGetMinMaxClockOfPState` """ @@ -23143,7 +24080,8 @@ cpdef device_set_clock_offsets(intptr_t device, intptr_t info): Args: device (intptr_t): The identifier of the target device. - info (intptr_t): Structure specifying the clock type (input), the pstate (input) and clock offset value (input). + info (intptr_t): Structure specifying the clock type (input), + the pstate (input) and clock offset value (input). .. seealso:: `nvmlDeviceSetClockOffsets` """ @@ -23159,7 +24097,8 @@ cpdef unsigned int device_get_power_management_limit(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the power management limit in milliwatts. + unsigned int: Reference in which to return the power + management limit in milliwatts. .. seealso:: `nvmlDeviceGetPowerManagementLimit` """ @@ -23179,8 +24118,10 @@ cpdef tuple device_get_power_management_limit_constraints(intptr_t device): Returns: A 2-tuple containing: - - unsigned int: Reference in which to return the minimum power management limit in milliwatts. - - unsigned int: Reference in which to return the maximum power management limit in milliwatts. + - unsigned int: Reference in which to return the minimum power + management limit in milliwatts. + - unsigned int: Reference in which to return the maximum power + management limit in milliwatts. .. seealso:: `nvmlDeviceGetPowerManagementLimitConstraints` """ @@ -23199,7 +24140,8 @@ cpdef unsigned int device_get_power_management_default_limit(intptr_t device) ex device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the default power management limit in milliwatts. + unsigned int: Reference in which to return the default power + management limit in milliwatts. .. seealso:: `nvmlDeviceGetPowerManagementDefaultLimit` """ @@ -23217,7 +24159,8 @@ cpdef unsigned int device_get_power_usage(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the power usage information. + unsigned int: Reference in which to return the power usage + information. .. seealso:: `nvmlDeviceGetPowerUsage` """ @@ -23235,7 +24178,8 @@ cpdef unsigned long long device_get_total_energy_consumption(intptr_t device) ex device (intptr_t): The identifier of the target device. Returns: - unsigned long long: Reference in which to return the energy consumption information. + unsigned long long: Reference in which to return the energy + consumption information. .. seealso:: `nvmlDeviceGetTotalEnergyConsumption` """ @@ -23253,7 +24197,8 @@ cpdef unsigned int device_get_enforced_power_limit(intptr_t device) except? 0: device (intptr_t): The device to communicate with. Returns: - unsigned int: Reference in which to return the power management limit in milliwatts. + unsigned int: Reference in which to return the power + management limit in milliwatts. .. seealso:: `nvmlDeviceGetEnforcedPowerLimit` """ @@ -23293,7 +24238,8 @@ cpdef object device_get_memory_info_v2(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlMemory_v2_t: Reference in which to return the memory information. + nvmlMemory_v2_t: Reference in which to return the memory + information. .. seealso:: `nvmlDeviceGetMemoryInfo_v2` """ @@ -23310,7 +24256,8 @@ cpdef int device_get_compute_mode(intptr_t device) except? -1: """Retrieves the current compute mode for the device or MIG device. Args: - device (intptr_t): The identifier of the target device handle or MIG device handle. + device (intptr_t): The identifier of the target device handle + or MIG device handle. Returns: int: Reference in which to return the current compute mode. @@ -23333,8 +24280,10 @@ cpdef tuple device_get_cuda_compute_capability(intptr_t device): Returns: A 2-tuple containing: - - int: Reference in which to return the major CUDA compute capability. - - int: Reference in which to return the minor CUDA compute capability. + - int: Reference in which to return the major CUDA compute + capability. + - int: Reference in which to return the minor CUDA compute + capability. .. seealso:: `nvmlDeviceGetCudaComputeCapability` """ @@ -23393,7 +24342,8 @@ cpdef unsigned int device_get_board_id(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return the device's board ID. + unsigned int: Reference in which to return the device's board + ID. .. seealso:: `nvmlDeviceGetBoardId` """ @@ -23411,7 +24361,9 @@ cpdef unsigned int device_get_multi_gpu_board(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return a zero or non-zero value to indicate whether the device is on a multi GPU board. + unsigned int: Reference in which to return a zero or non-zero + value to indicate whether the device is on a multi GPU + board. .. seealso:: `nvmlDeviceGetMultiGpuBoard` """ @@ -23427,11 +24379,14 @@ cpdef unsigned long long device_get_total_ecc_errors(intptr_t device, int error_ Args: device (intptr_t): The identifier of the target device. - error_type (MemoryErrorType): Flag that specifies the type of the errors. - counter_type (EccCounterType): Flag that specifies the counter-type of the errors. + error_type (MemoryErrorType): Flag that specifies the type of + the errors. + counter_type (EccCounterType): Flag that specifies the + counter-type of the errors. Returns: - unsigned long long: Reference in which to return the specified ECC errors. + unsigned long long: Reference in which to return the specified + ECC errors. .. seealso:: `nvmlDeviceGetTotalEccErrors` """ @@ -23447,12 +24402,16 @@ cpdef unsigned long long device_get_memory_error_counter(intptr_t device, int er Args: device (intptr_t): The identifier of the target device. - error_type (MemoryErrorType): Flag that specifies the type of error. - counter_type (EccCounterType): Flag that specifies the counter-type of the errors. - location_type (MemoryLocation): Specifies the location of the counter. + error_type (MemoryErrorType): Flag that specifies the type of + error. + counter_type (EccCounterType): Flag that specifies the + counter-type of the errors. + location_type (MemoryLocation): Specifies the location of the + counter. Returns: - unsigned long long: Reference in which to return the ECC counter. + unsigned long long: Reference in which to return the ECC + counter. .. seealso:: `nvmlDeviceGetMemoryErrorCounter` """ @@ -23470,7 +24429,8 @@ cpdef object device_get_utilization_rates(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlUtilization_t: Reference in which to return the utilization information. + nvmlUtilization_t: Reference in which to return the + utilization information. .. seealso:: `nvmlDeviceGetUtilizationRates` """ @@ -23491,8 +24451,10 @@ cpdef tuple device_get_encoder_utilization(intptr_t device): Returns: A 2-tuple containing: - - unsigned int: Reference to an unsigned int for encoder utilization info. - - unsigned int: Reference to an unsigned int for the sampling period in US. + - unsigned int: Reference to an unsigned int for encoder + utilization info. + - unsigned int: Reference to an unsigned int for the sampling + period in US. .. seealso:: `nvmlDeviceGetEncoderUtilization` """ @@ -23512,7 +24474,8 @@ cpdef unsigned int device_get_encoder_capacity(intptr_t device, int encoder_quer encoder_query_type (EncoderType): Type of encoder to query. Returns: - unsigned int: Reference to an unsigned int for the encoder capacity. + unsigned int: Reference to an unsigned int for the encoder + capacity. .. seealso:: `nvmlDeviceGetEncoderCapacity` """ @@ -23532,9 +24495,12 @@ cpdef tuple device_get_encoder_stats(intptr_t device): Returns: A 3-tuple containing: - - unsigned int: Reference to an unsigned int for count of active encoder sessions. - - unsigned int: Reference to an unsigned int for trailing average FPS of all active sessions. - - unsigned int: Reference to an unsigned int for encode latency in microseconds. + - unsigned int: Reference to an unsigned int for count of active + encoder sessions. + - unsigned int: Reference to an unsigned int for trailing + average FPS of all active sessions. + - unsigned int: Reference to an unsigned int for encode latency + in microseconds. .. seealso:: `nvmlDeviceGetEncoderStats` """ @@ -23554,7 +24520,8 @@ cpdef object device_get_encoder_sessions(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlEncoderSessionInfo_t: Reference in which to return the session information. + nvmlEncoderSessionInfo_t: Reference in which to return the + session information. .. seealso:: `nvmlDeviceGetEncoderSessions` """ @@ -23581,8 +24548,10 @@ cpdef tuple device_get_decoder_utilization(intptr_t device): Returns: A 2-tuple containing: - - unsigned int: Reference to an unsigned int for decoder utilization info. - - unsigned int: Reference to an unsigned int for the sampling period in US. + - unsigned int: Reference to an unsigned int for decoder + utilization info. + - unsigned int: Reference to an unsigned int for the sampling + period in US. .. seealso:: `nvmlDeviceGetDecoderUtilization` """ @@ -23603,8 +24572,10 @@ cpdef tuple device_get_jpg_utilization(intptr_t device): Returns: A 2-tuple containing: - - unsigned int: Reference to an unsigned int for jpg utilization info. - - unsigned int: Reference to an unsigned int for the sampling period in US. + - unsigned int: Reference to an unsigned int for jpg utilization + info. + - unsigned int: Reference to an unsigned int for the sampling + period in US. .. seealso:: `nvmlDeviceGetJpgUtilization` """ @@ -23625,8 +24596,10 @@ cpdef tuple device_get_ofa_utilization(intptr_t device): Returns: A 2-tuple containing: - - unsigned int: Reference to an unsigned int for ofa utilization info. - - unsigned int: Reference to an unsigned int for the sampling period in US. + - unsigned int: Reference to an unsigned int for ofa utilization + info. + - unsigned int: Reference to an unsigned int for the sampling + period in US. .. seealso:: `nvmlDeviceGetOfaUtilization` """ @@ -23645,7 +24618,8 @@ cpdef object device_get_fbc_stats(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlFBCStats_t: Reference to ``nvmlFBCStats_t`` structure containing NvFBC stats. + nvmlFBCStats_t: Reference to ``nvmlFBCStats_t`` structure + containing NvFBC stats. .. seealso:: `nvmlDeviceGetFBCStats` """ @@ -23664,7 +24638,8 @@ cpdef object device_get_fbc_sessions(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlFBCSessionInfo_t: Reference in which to return the session information. + nvmlFBCSessionInfo_t: Reference in which to return the session + information. .. seealso:: `nvmlDeviceGetFBCSessions` """ @@ -23730,7 +24705,8 @@ cpdef object device_get_bridge_chip_info(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlBridgeChipHierarchy_t: Reference to the returned bridge chip Hierarchy. + nvmlBridgeChipHierarchy_t: Reference to the returned bridge + chip Hierarchy. .. seealso:: `nvmlDeviceGetBridgeChipInfo` """ @@ -23749,7 +24725,8 @@ cpdef object device_get_compute_running_processes_v3(intptr_t device): device (intptr_t): The device handle or MIG device handle. Returns: - nvmlProcessInfo_t: Reference in which to return the process information. + nvmlProcessInfo_t: Reference in which to return the process + information. .. seealso:: `nvmlDeviceGetComputeRunningProcesses_v3` """ @@ -23774,7 +24751,8 @@ cpdef object device_get_graphics_running_processes_v3(intptr_t device): device (intptr_t): The device handle or MIG device handle. Returns: - nvmlProcessInfo_t: Reference in which to return the process information. + nvmlProcessInfo_t: Reference in which to return the process + information. .. seealso:: `nvmlDeviceGetGraphicsRunningProcesses_v3` """ @@ -23799,7 +24777,8 @@ cpdef object device_get_mps_compute_running_processes_v3(intptr_t device): device (intptr_t): The device handle or MIG device handle. Returns: - nvmlProcessInfo_t: Reference in which to return the process information. + nvmlProcessInfo_t: Reference in which to return the process + information. .. seealso:: `nvmlDeviceGetMPSComputeRunningProcesses_v3` """ @@ -23825,7 +24804,8 @@ cpdef int device_on_same_board(intptr_t device1, intptr_t device2) except? 0: device2 (intptr_t): The second GPU device. Returns: - int: Reference in which to return the status. Non-zero indicates that the GPUs are on the same board. + int: Reference in which to return the status. Non-zero + indicates that the GPUs are on the same board. .. seealso:: `nvmlDeviceOnSameBoard` """ @@ -23844,7 +24824,10 @@ cpdef int device_get_api_restriction(intptr_t device, int api_type) except? -1: api_type (RestrictedAPI): Target API type for this operation. Returns: - int: Reference in which to return the current restriction NVML_FEATURE_ENABLED indicates that the API is root-only NVML_FEATURE_DISABLED indicates that the API is accessible to all users. + int: Reference in which to return the current restriction + NVML_FEATURE_ENABLED indicates that the API is root-only + NVML_FEATURE_DISABLED indicates that the API is accessible + to all users. .. seealso:: `nvmlDeviceGetAPIRestriction` """ @@ -23862,7 +24845,8 @@ cpdef object device_get_bar1_memory_info(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlBAR1Memory_t: Reference in which BAR1 memory information is returned. + nvmlBAR1Memory_t: Reference in which BAR1 memory information + is returned. .. seealso:: `nvmlDeviceGetBAR1MemoryInfo` """ @@ -23881,7 +24865,8 @@ cpdef unsigned int device_get_irq_num(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: The interrupt number associated with the specified device. + unsigned int: The interrupt number associated with the + specified device. .. seealso:: `nvmlDeviceGetIrqNum` """ @@ -23989,7 +24974,9 @@ cpdef unsigned int device_get_adaptive_clock_info_status(intptr_t device) except device (intptr_t): The identifier of the target device. Returns: - unsigned int: The current adaptive clocking status, either NVML_ADAPTIVE_CLOCKING_INFO_STATUS_DISABLED or NVML_ADAPTIVE_CLOCKING_INFO_STATUS_ENABLED. + unsigned int: The current adaptive clocking status, either + NVML_ADAPTIVE_CLOCKING_INFO_STATUS_DISABLED or + NVML_ADAPTIVE_CLOCKING_INFO_STATUS_ENABLED. .. seealso:: `nvmlDeviceGetAdaptiveClockInfoStatus` """ @@ -24057,7 +25044,8 @@ cpdef object device_get_conf_compute_mem_size_info(intptr_t device): device (intptr_t): Device handle. Returns: - nvmlConfComputeMemSizeInfo_t: Protected/Unprotected Memory sizes. + nvmlConfComputeMemSizeInfo_t: Protected/Unprotected Memory + sizes. .. seealso:: `nvmlDeviceGetConfComputeMemSizeInfo` """ @@ -24073,7 +25061,9 @@ cpdef unsigned int system_get_conf_compute_gpus_ready_state() except? 0: """Get Conf Computing GPUs ready state. Returns: - unsigned int: Returns GPU current work accepting state, NVML_CC_ACCEPTING_CLIENT_REQUESTS_TRUE or NVML_CC_ACCEPTING_CLIENT_REQUESTS_FALSE. + unsigned int: Returns GPU current work accepting state, + NVML_CC_ACCEPTING_CLIENT_REQUESTS_TRUE or + NVML_CC_ACCEPTING_CLIENT_REQUESTS_FALSE. .. seealso:: `nvmlSystemGetConfComputeGpusReadyState` """ @@ -24091,7 +25081,8 @@ cpdef object device_get_conf_compute_protected_memory_usage(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlMemory_t: Reference in which to return the memory information. + nvmlMemory_t: Reference in which to return the memory + information. .. seealso:: `nvmlDeviceGetConfComputeProtectedMemoryUsage` """ @@ -24110,7 +25101,8 @@ cpdef object device_get_conf_compute_gpu_certificate(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlConfComputeGpuCertificate_t: Reference in which to return the gpu certificate information. + nvmlConfComputeGpuCertificate_t: Reference in which to return + the gpu certificate information. .. seealso:: `nvmlDeviceGetConfComputeGpuCertificate` """ @@ -24127,7 +25119,8 @@ cpdef device_set_conf_compute_unprotected_mem_size(intptr_t device, unsigned lon Args: device (intptr_t): Device Handle. - size_ki_b (unsigned long long): Unprotected Memory size to be set in KiB. + size_ki_b (unsigned long long): Unprotected Memory size to be + set in KiB. .. seealso:: `nvmlDeviceSetConfComputeUnprotectedMemSize` """ @@ -24140,7 +25133,9 @@ cpdef system_set_conf_compute_gpus_ready_state(unsigned int is_accepting_work): """Set Conf Computing GPUs ready state. Args: - is_accepting_work (unsigned int): GPU accepting new work, NVML_CC_ACCEPTING_CLIENT_REQUESTS_TRUE or NVML_CC_ACCEPTING_CLIENT_REQUESTS_FALSE. + is_accepting_work (unsigned int): GPU accepting new work, + NVML_CC_ACCEPTING_CLIENT_REQUESTS_TRUE or + NVML_CC_ACCEPTING_CLIENT_REQUESTS_FALSE. .. seealso:: `nvmlSystemSetConfComputeGpusReadyState` """ @@ -24194,7 +25189,8 @@ cpdef tuple device_get_gsp_firmware_mode(intptr_t device): A 2-tuple containing: - unsigned int: Pointer to specify if GSP firmware is enabled. - - unsigned int: Pointer to specify if GSP firmware is supported by default on ``device``. + - unsigned int: Pointer to specify if GSP firmware is supported + by default on ``device``. .. seealso:: `nvmlDeviceGetGspFirmwareMode` """ @@ -24249,10 +25245,12 @@ cpdef object device_get_accounting_stats(intptr_t device, unsigned int pid): Args: device (intptr_t): The identifier of the target device. - pid (unsigned int): Process Id of the target process to query stats for. + pid (unsigned int): Process Id of the target process to query + stats for. Returns: - nvmlAccountingStats_t: Reference in which to return the process's accounting stats. + nvmlAccountingStats_t: Reference in which to return the + process's accounting stats. .. seealso:: `nvmlDeviceGetAccountingStats` """ @@ -24271,7 +25269,8 @@ cpdef object device_get_accounting_pids(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to return list of process ids. + unsigned int: Reference in which to return list of process + ids. .. seealso:: `nvmlDeviceGetAccountingPids` """ @@ -24296,7 +25295,9 @@ cpdef unsigned int device_get_accounting_buffer_size(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference in which to provide the size (in number of elements) of the circular buffer for accounting stats. + unsigned int: Reference in which to provide the size (in + number of elements) of the circular buffer for accounting + stats. .. seealso:: `nvmlDeviceGetAccountingBufferSize` """ @@ -24312,7 +25313,8 @@ cpdef object device_get_retired_pages(intptr_t device, int cause): Args: device (intptr_t): The identifier of the target device. - cause (PageRetirementCause): Filter page addresses by cause of retirement. + cause (PageRetirementCause): Filter page addresses by cause of + retirement. Returns: unsigned long long: Buffer to write the page addresses into. @@ -24360,10 +25362,14 @@ cpdef tuple device_get_remapped_rows(intptr_t device): Returns: A 4-tuple containing: - - unsigned int: Reference for number of rows remapped due to correctable errors. - - unsigned int: Reference for number of rows remapped due to uncorrectable errors. - - unsigned int: Reference for whether or not remappings are pending. - - unsigned int: Reference that is set when a remapping has failed in the past. + - unsigned int: Reference for number of rows remapped due to + correctable errors. + - unsigned int: Reference for number of rows remapped due to + uncorrectable errors. + - unsigned int: Reference for whether or not remappings are + pending. + - unsigned int: Reference that is set when a remapping has + failed in the past. .. seealso:: `nvmlDeviceGetRemappedRows` """ @@ -24403,7 +25409,8 @@ cpdef unsigned int device_get_architecture(intptr_t device) except? 0: device (intptr_t): The identifier of the target device. Returns: - unsigned int: Reference where architecture is returned, if call successful. Set to NVML_DEVICE_ARCH_* upon success. + unsigned int: Reference where architecture is returned, if + call successful. Set to NVML_DEVICE_ARCH_* upon success. .. seealso:: `nvmlDeviceGetArchitecture` """ @@ -24421,7 +25428,8 @@ cpdef object device_get_clk_mon_status(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlClkMonStatus_t: Reference in which to return the clkmon fault status. + nvmlClkMonStatus_t: Reference in which to return the clkmon + fault status. .. seealso:: `nvmlDeviceGetClkMonStatus` """ @@ -24438,10 +25446,13 @@ cpdef object device_get_process_utilization(intptr_t device, unsigned long long Args: device (intptr_t): The identifier of the target device. - last_seen_time_stamp (unsigned long long): Return only samples with timestamp greater than last_seen_time_stamp. + last_seen_time_stamp (unsigned long long): Return only samples + with timestamp greater than last_seen_time_stamp. Returns: - nvmlProcessUtilizationSample_t: Pointer to caller-supplied buffer in which guest process utilization samples are returned. + nvmlProcessUtilizationSample_t: Pointer to caller-supplied + buffer in which guest process utilization samples are + returned. .. seealso:: `nvmlDeviceGetProcessUtilization` """ @@ -24491,7 +25502,8 @@ cpdef device_set_compute_mode(intptr_t device, int mode): """Set the compute mode for the device or MIG device. Args: - device (intptr_t): The identifier of the target device handle or MIG device handle. + device (intptr_t): The identifier of the target device handle + or MIG device handle. mode (ComputeMode): The target compute mode. .. seealso:: `nvmlDeviceSetComputeMode` @@ -24520,7 +25532,8 @@ cpdef device_clear_ecc_error_counts(intptr_t device, int counter_type): Args: device (intptr_t): The identifier of the target device. - counter_type (EccCounterType): Flag that indicates which type of errors should be cleared. + counter_type (EccCounterType): Flag that indicates which type + of errors should be cleared. .. seealso:: `nvmlDeviceClearEccErrorCounts` """ @@ -24549,8 +25562,10 @@ cpdef device_set_gpu_locked_clocks(intptr_t device, unsigned int min_gpu_clock_m Args: device (intptr_t): The identifier of the target device. - min_gpu_clock_m_hz (unsigned int): Requested minimum gpu clock in MHz. - max_gpu_clock_m_hz (unsigned int): Requested maximum gpu clock in MHz. + min_gpu_clock_m_hz (unsigned int): Requested minimum gpu clock + in MHz. + max_gpu_clock_m_hz (unsigned int): Requested maximum gpu clock + in MHz. .. seealso:: `nvmlDeviceSetGpuLockedClocks` """ @@ -24577,8 +25592,10 @@ cpdef device_set_memory_locked_clocks(intptr_t device, unsigned int min_mem_cloc Args: device (intptr_t): The identifier of the target device. - min_mem_clock_m_hz (unsigned int): Requested minimum memory clock in MHz. - max_mem_clock_m_hz (unsigned int): Requested maximum memory clock in MHz. + min_mem_clock_m_hz (unsigned int): Requested minimum memory + clock in MHz. + max_mem_clock_m_hz (unsigned int): Requested maximum memory + clock in MHz. .. seealso:: `nvmlDeviceSetMemoryLockedClocks` """ @@ -24605,7 +25622,8 @@ cpdef device_set_auto_boosted_clocks_enabled(intptr_t device, int enabled): Args: device (intptr_t): The identifier of the target device. - enabled (EnableState): What state to try to set Auto Boosted clocks of the target device to. + enabled (EnableState): What state to try to set Auto Boosted + clocks of the target device to. .. seealso:: `nvmlDeviceSetAutoBoostedClocksEnabled` """ @@ -24619,8 +25637,10 @@ cpdef device_set_default_auto_boosted_clocks_enabled(intptr_t device, int enable Args: device (intptr_t): The identifier of the target device. - enabled (EnableState): What state to try to set default Auto Boosted clocks of the target device to. - flags (unsigned int): Flags that change the default behavior. Currently Unused. + enabled (EnableState): What state to try to set default Auto + Boosted clocks of the target device to. + flags (unsigned int): Flags that change the default behavior. + Currently Unused. .. seealso:: `nvmlDeviceSetDefaultAutoBoostedClocksEnabled` """ @@ -24693,7 +25713,8 @@ cpdef device_set_fan_speed_v2(intptr_t device, unsigned int fan, unsigned int sp Args: device (intptr_t): The identifier of the target device. fan (unsigned int): The index of the fan, starting at zero. - speed (unsigned int): The target speed of the fan [0-100] in % of max speed. + speed (unsigned int): The target speed of the fan [0-100] in % + of max speed. .. seealso:: `nvmlDeviceSetFanSpeed_v2` """ @@ -24737,7 +25758,9 @@ cpdef int device_get_nvlink_state(intptr_t device, unsigned int link) except? -1 link (unsigned int): Specifies the NvLink link to be queried. Returns: - int: ``nvmlEnableState_t`` where NVML_FEATURE_ENABLED indicates that the link is active and NVML_FEATURE_DISABLED indicates it is inactive. + int: ``nvmlEnableState_t`` where NVML_FEATURE_ENABLED + indicates that the link is active and + NVML_FEATURE_DISABLED indicates it is inactive. .. seealso:: `nvmlDeviceGetNvLinkState` """ @@ -24756,7 +25779,8 @@ cpdef unsigned int device_get_nvlink_version(intptr_t device, unsigned int link) link (unsigned int): Specifies the NvLink link to be queried. Returns: - unsigned int: Requested NvLink version from ``nvmlNvlinkVersion_t``. + unsigned int: Requested NvLink version from + ``nvmlNvlinkVersion_t``. .. seealso:: `nvmlDeviceGetNvLinkVersion` """ @@ -24773,10 +25797,12 @@ cpdef unsigned int device_get_nvlink_capability(intptr_t device, unsigned int li Args: device (intptr_t): The identifier of the target device. link (unsigned int): Specifies the NvLink link to be queried. - capability (NvLinkCapability): Specifies the ``nvmlNvLinkCapability_t`` to be queried. + capability (NvLinkCapability): Specifies the + ``nvmlNvLinkCapability_t`` to be queried. Returns: - unsigned int: A boolean for the queried capability indicating that feature is available. + unsigned int: A boolean for the queried capability indicating + that feature is available. .. seealso:: `nvmlDeviceGetNvLinkCapability` """ @@ -24795,7 +25821,8 @@ cpdef object device_get_nvlink_remote_pci_info_v2(intptr_t device, unsigned int link (unsigned int): Specifies the NvLink link to be queried. Returns: - nvmlPciInfo_t: ``nvmlPciInfo_t`` of the remote node for the specified link. + nvmlPciInfo_t: ``nvmlPciInfo_t`` of the remote node for the + specified link. .. seealso:: `nvmlDeviceGetNvLinkRemotePciInfo_v2` """ @@ -24813,7 +25840,8 @@ cpdef unsigned long long device_get_nvlink_error_counter(intptr_t device, unsign Args: device (intptr_t): The identifier of the target device. link (unsigned int): Specifies the NvLink link to be queried. - counter (NvLinkErrorCounter): Specifies the NvLink counter to be queried. + counter (NvLinkErrorCounter): Specifies the NvLink counter to + be queried. Returns: unsigned long long: Returned counter value. @@ -24849,7 +25877,8 @@ cpdef int device_get_nvlink_remote_device_type(intptr_t device, unsigned int lin link (unsigned int): The NVLink link index on the target GPU. Returns: - int: Pointer in which the output remote device type is returned. + int: Pointer in which the output remote device type is + returned. .. seealso:: `nvmlDeviceGetNvLinkRemoteDeviceType` """ @@ -24895,7 +25924,8 @@ cpdef object device_get_nvlink_supported_bw_modes(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlNvlinkSupportedBwModes_v1_t: Reference to ``nvmlNvlinkSupportedBwModes_t``. + nvmlNvlinkSupportedBwModes_v1_t: Reference to + ``nvmlNvlinkSupportedBwModes_t``. .. seealso:: `nvmlDeviceGetNvlinkSupportedBwModes` """ @@ -24915,7 +25945,8 @@ cpdef object device_get_nvlink_bw_mode(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlNvlinkGetBwMode_v1_t: Reference to ``nvmlNvlinkGetBwMode_t``. + nvmlNvlinkGetBwMode_v1_t: Reference to + ``nvmlNvlinkGetBwMode_t``. .. seealso:: `nvmlDeviceGetNvlinkBwMode` """ @@ -24933,7 +25964,8 @@ cpdef device_set_nvlink_bw_mode(intptr_t device, intptr_t set_bw_mode): Args: device (intptr_t): The identifier of the target device. - set_bw_mode (intptr_t): Reference to ``nvmlNvlinkSetBwMode_t``. + set_bw_mode (intptr_t): Reference to + ``nvmlNvlinkSetBwMode_t``. .. seealso:: `nvmlDeviceSetNvlinkBwMode` """ @@ -24963,7 +25995,8 @@ cpdef device_register_events(intptr_t device, unsigned long long event_types, in Args: device (intptr_t): The identifier of the target device. - event_types (unsigned long long): Bitmask of ``Event Types`` to record. + event_types (unsigned long long): Bitmask of ``Event Types`` + to record. set (intptr_t): Set to which add new event types. .. seealso:: `nvmlDeviceRegisterEvents` @@ -24980,7 +26013,8 @@ cpdef unsigned long long device_get_supported_event_types(intptr_t device) excep device (intptr_t): The identifier of the target device. Returns: - unsigned long long: Reference in which to return bitmask of supported events. + unsigned long long: Reference in which to return bitmask of + supported events. .. seealso:: `nvmlDeviceGetSupportedEventTypes` """ @@ -24996,7 +26030,8 @@ cpdef object event_set_wait_v2(intptr_t set, unsigned int timeoutms): Args: set (intptr_t): Reference to set of events to wait on. - timeoutms (unsigned int): Maximum amount of wait time in milliseconds for registered event. + timeoutms (unsigned int): Maximum amount of wait time in + milliseconds for registered event. Returns: nvmlEventData_t: Reference in which to return event data. @@ -25028,8 +26063,10 @@ cpdef device_modify_drain_state(intptr_t pci_info, int new_state): """Modify the drain state of a GPU. This method forces a GPU to no longer accept new incoming requests. Any new NVML process will no longer see this GPU. Persistence mode for this GPU must be turned off before this call is made. Must be called as administrator. For Linux only. Args: - pci_info (intptr_t): The PCI address of the GPU drain state to be modified. - new_state (EnableState): The drain state that should be entered, see ``nvmlEnableState_t``. + pci_info (intptr_t): The PCI address of the GPU drain state to + be modified. + new_state (EnableState): The drain state that should be + entered, see ``nvmlEnableState_t``. .. seealso:: `nvmlDeviceModifyDrainState` """ @@ -25042,10 +26079,12 @@ cpdef int device_query_drain_state(intptr_t pci_info) except? -1: """Query the drain state of a GPU. This method is used to check if a GPU is in a currently draining state. For Linux only. Args: - pci_info (intptr_t): The PCI address of the GPU drain state to be queried. + pci_info (intptr_t): The PCI address of the GPU drain state to + be queried. Returns: - int: The current drain state for this GPU, see ``nvmlEnableState_t``. + int: The current drain state for this GPU, see + ``nvmlEnableState_t``. .. seealso:: `nvmlDeviceQueryDrainState` """ @@ -25061,8 +26100,10 @@ cpdef device_remove_gpu_v2(intptr_t pci_info, int gpu_state, int link_state): Args: pci_info (intptr_t): The PCI address of the GPU to be removed. - gpu_state (DetachGpuState): Whether the GPU is to be removed, from the OS see ``nvmlDetachGpuState_t``. - link_state (PcieLinkState): Requested upstream PCIe link state, see ``nvmlPcieLinkState_t``. + gpu_state (DetachGpuState): Whether the GPU is to be removed, + from the OS see ``nvmlDetachGpuState_t``. + link_state (PcieLinkState): Requested upstream PCIe link + state, see ``nvmlPcieLinkState_t``. .. seealso:: `nvmlDeviceRemoveGpu_v2` """ @@ -25075,7 +26116,8 @@ cpdef device_discover_gpus(intptr_t pci_info): """Request the OS and the NVIDIA kernel driver to rediscover a portion of the PCI subsystem looking for GPUs that were previously removed. The portion of the PCI tree can be narrowed by specifying a domain, bus, and device. If all are zeroes then the entire PCI tree will be searched. Please note that for long-running NVML processes the enumeration will change based on how many GPUs are discovered and where they are inserted in bus order. Args: - pci_info (intptr_t): The PCI tree to be searched. Only the domain, bus, and device fields are used in this call. + pci_info (intptr_t): The PCI tree to be searched. Only the + domain, bus, and device fields are used in this call. .. seealso:: `nvmlDeviceDiscoverGpus` """ @@ -25091,7 +26133,8 @@ cpdef int device_get_virtualization_mode(intptr_t device) except? -1: device (intptr_t): Identifier of the target device. Returns: - int: Reference to virtualization mode. One of NVML_GPU_VIRTUALIZATION_?. + int: Reference to virtualization mode. One of + ``NVML_GPU_VIRTUALIZATION_?``. .. seealso:: `nvmlDeviceGetVirtualizationMode` """ @@ -25125,7 +26168,8 @@ cpdef device_set_virtualization_mode(intptr_t device, int virtual_mode): Args: device (intptr_t): Identifier of the target device. - virtual_mode (GpuVirtualizationMode): virtualization mode. One of NVML_GPU_VIRTUALIZATION_?. + virtual_mode (GpuVirtualizationMode): virtualization mode. One + of ``NVML_GPU_VIRTUALIZATION_?``. .. seealso:: `nvmlDeviceSetVirtualizationMode` """ @@ -25141,7 +26185,8 @@ cpdef unsigned long long vgpu_type_get_gsp_heap_size(unsigned int vgpu_type_id) vgpu_type_id (unsigned int): Handle to vGPU type. Returns: - unsigned long long: Reference to return the GSP heap size value. + unsigned long long: Reference to return the GSP heap size + value. .. seealso:: `nvmlVgpuTypeGetGspHeapSize` """ @@ -25159,7 +26204,8 @@ cpdef unsigned long long vgpu_type_get_fb_reservation(unsigned int vgpu_type_id) vgpu_type_id (unsigned int): Handle to vGPU type. Returns: - unsigned long long: Reference to return the framebuffer reservation. + unsigned long long: Reference to return the framebuffer + reservation. .. seealso:: `nvmlVgpuTypeGetFbReservation` """ @@ -25175,7 +26221,8 @@ cpdef device_set_vgpu_capabilities(intptr_t device, int capability, int state): Args: device (intptr_t): The identifier of the target device. - capability (DeviceVgpuCapability): Specifies the ``nvmlDeviceVgpuCapability_t`` to be set. + capability (DeviceVgpuCapability): Specifies the + ``nvmlDeviceVgpuCapability_t`` to be set. state (EnableState): The target capability mode. .. seealso:: `nvmlDeviceSetVgpuCapabilities` @@ -25192,7 +26239,8 @@ cpdef object device_get_grid_licensable_features_v4(intptr_t device): device (intptr_t): Identifier of the target device. Returns: - nvmlGridLicensableFeatures_t: Pointer to structure in which vGPU software licensable features are returned. + nvmlGridLicensableFeatures_t: Pointer to structure in which + vGPU software licensable features are returned. .. seealso:: `nvmlDeviceGetGridLicensableFeatures_v4` """ @@ -25208,10 +26256,12 @@ cpdef unsigned int get_vgpu_driver_capabilities(int capability) except? 0: """Retrieve the requested vGPU driver capability. Args: - capability (VgpuDriverCapability): Specifies the ``nvmlVgpuDriverCapability_t`` to be queried. + capability (VgpuDriverCapability): Specifies the + ``nvmlVgpuDriverCapability_t`` to be queried. Returns: - unsigned int: A boolean for the queried capability indicating that feature is supported. + unsigned int: A boolean for the queried capability indicating + that feature is supported. .. seealso:: `nvmlGetVgpuDriverCapabilities` """ @@ -25227,10 +26277,12 @@ cpdef unsigned int device_get_vgpu_capabilities(intptr_t device, int capability) Args: device (intptr_t): The identifier of the target device. - capability (DeviceVgpuCapability): Specifies the ``nvmlDeviceVgpuCapability_t`` to be queried. + capability (DeviceVgpuCapability): Specifies the + ``nvmlDeviceVgpuCapability_t`` to be queried. Returns: - unsigned int: Specifies that the queried capability is supported, and also returns capability's data. + unsigned int: Specifies that the queried capability is + supported, and also returns capability's data. .. seealso:: `nvmlDeviceGetVgpuCapabilities` """ @@ -25293,8 +26345,10 @@ cpdef tuple vgpu_type_get_device_id(unsigned int vgpu_type_id): Returns: A 2-tuple containing: - - unsigned long long: Device ID and vendor ID of the device contained in single 32 bit value. - - unsigned long long: Subsystem ID and subsystem vendor ID of the device contained in single 32 bit value. + - unsigned long long: Device ID and vendor ID of the device + contained in single 32 bit value. + - unsigned long long: Subsystem ID and subsystem vendor ID of + the device contained in single 32 bit value. .. seealso:: `nvmlVgpuTypeGetDeviceID` """ @@ -25347,13 +26401,16 @@ cpdef tuple vgpu_type_get_resolution(unsigned int vgpu_type_id, unsigned int dis Args: vgpu_type_id (unsigned int): Handle to vGPU type. - display_index (unsigned int): Zero-based index of display head. + display_index (unsigned int): Zero-based index of display + head. Returns: A 2-tuple containing: - - unsigned int: Pointer to maximum number of pixels in X dimension. - - unsigned int: Pointer to maximum number of pixels in Y dimension. + - unsigned int: Pointer to maximum number of pixels in X + dimension. + - unsigned int: Pointer to maximum number of pixels in Y + dimension. .. seealso:: `nvmlVgpuTypeGetResolution` """ @@ -25410,7 +26467,8 @@ cpdef unsigned int vgpu_type_get_max_instances(intptr_t device, unsigned int vgp vgpu_type_id (unsigned int): Handle to vGPU type. Returns: - unsigned int: Pointer to get the max number of vGPU instances that can be created on a deicve for given vgpu_type_id. + unsigned int: Pointer to get the max number of vGPU instances + that can be created on a deicve for given vgpu_type_id. .. seealso:: `nvmlVgpuTypeGetMaxInstances` """ @@ -25428,7 +26486,8 @@ cpdef unsigned int vgpu_type_get_max_instances_per_vm(unsigned int vgpu_type_id) vgpu_type_id (unsigned int): Handle to vGPU type. Returns: - unsigned int: Pointer to get the max number of vGPU instances supported per VM for given ``vgpu_type_id``. + unsigned int: Pointer to get the max number of vGPU instances + supported per VM for given ``vgpu_type_id``. .. seealso:: `nvmlVgpuTypeGetMaxInstancesPerVm` """ @@ -25446,7 +26505,8 @@ cpdef object vgpu_type_get_bar1_info(unsigned int vgpu_type_id): vgpu_type_id (unsigned int): Handle to vGPU type. Returns: - nvmlVgpuTypeBar1Info_v1_t: Pointer to the vGPU type BAR1 information structure ``nvmlVgpuTypeBar1Info_t``. + nvmlVgpuTypeBar1Info_v1_t: Pointer to the vGPU type BAR1 + information structure ``nvmlVgpuTypeBar1Info_t``. .. seealso:: `nvmlVgpuTypeGetBAR1Info` """ @@ -25463,7 +26523,8 @@ cpdef str vgpu_instance_get_uuid(unsigned int vgpu_instance): """Retrieve the UUID of a vGPU instance. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: char: Pointer to caller-supplied buffer to hold vGPU UUID. @@ -25482,7 +26543,8 @@ cpdef str vgpu_instance_get_vm_driver_version(unsigned int vgpu_instance): """Retrieve the NVIDIA driver version installed in the VM associated with a vGPU. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: char: Caller-supplied buffer to return driver version string. @@ -25501,7 +26563,8 @@ cpdef unsigned long long vgpu_instance_get_fb_usage(unsigned int vgpu_instance) """Retrieve the framebuffer usage in bytes. Args: - vgpu_instance (unsigned int): The identifier of the target instance. + vgpu_instance (unsigned int): The identifier of the target + instance. Returns: unsigned long long: Pointer to framebuffer usage in bytes. @@ -25519,7 +26582,8 @@ cpdef unsigned int vgpu_instance_get_license_status(unsigned int vgpu_instance) """[Deprecated]. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: unsigned int: Reference to return the licensing status. @@ -25537,7 +26601,8 @@ cpdef unsigned int vgpu_instance_get_type(unsigned int vgpu_instance) except? 0: """Retrieve the vGPU type of a vGPU instance. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: unsigned int: Reference to return the vgpu_type_id. @@ -25555,7 +26620,8 @@ cpdef unsigned int vgpu_instance_get_frame_rate_limit(unsigned int vgpu_instance """Retrieve the frame rate limit set for the vGPU instance. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: unsigned int: Reference to return the frame rate limit. @@ -25573,7 +26639,8 @@ cpdef int vgpu_instance_get_ecc_mode(unsigned int vgpu_instance) except? -1: """Retrieve the current ECC mode of vGPU instance. Args: - vgpu_instance (unsigned int): The identifier of the target vGPU instance. + vgpu_instance (unsigned int): The identifier of the target + vGPU instance. Returns: int: Reference in which to return the current ECC mode. @@ -25591,10 +26658,12 @@ cpdef unsigned int vgpu_instance_get_encoder_capacity(unsigned int vgpu_instance """Retrieve the encoder capacity of a vGPU instance, as a percentage of maximum encoder capacity with valid values in the range 0-100. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: - unsigned int: Reference to an unsigned int for the encoder capacity. + unsigned int: Reference to an unsigned int for the encoder + capacity. .. seealso:: `nvmlVgpuInstanceGetEncoderCapacity` """ @@ -25609,8 +26678,10 @@ cpdef vgpu_instance_set_encoder_capacity(unsigned int vgpu_instance, unsigned in """Set the encoder capacity of a vGPU instance, as a percentage of maximum encoder capacity with valid values in the range 0-100. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. - encoder_capacity (unsigned int): Unsigned int for the encoder capacity value. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. + encoder_capacity (unsigned int): Unsigned int for the encoder + capacity value. .. seealso:: `nvmlVgpuInstanceSetEncoderCapacity` """ @@ -25623,14 +26694,18 @@ cpdef tuple vgpu_instance_get_encoder_stats(unsigned int vgpu_instance): """Retrieves the current encoder statistics of a vGPU Instance. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: A 3-tuple containing: - - unsigned int: Reference to an unsigned int for count of active encoder sessions. - - unsigned int: Reference to an unsigned int for trailing average FPS of all active sessions. - - unsigned int: Reference to an unsigned int for encode latency in microseconds. + - unsigned int: Reference to an unsigned int for count of active + encoder sessions. + - unsigned int: Reference to an unsigned int for trailing + average FPS of all active sessions. + - unsigned int: Reference to an unsigned int for encode latency + in microseconds. .. seealso:: `nvmlVgpuInstanceGetEncoderStats` """ @@ -25647,10 +26722,12 @@ cpdef object vgpu_instance_get_encoder_sessions(unsigned int vgpu_instance): """Retrieves information about all active encoder sessions on a vGPU Instance. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: - nvmlEncoderSessionInfo_t: Reference to caller supplied array in which the list of session information us returned. + nvmlEncoderSessionInfo_t: Reference to caller supplied array + in which the list of session information us returned. .. seealso:: `nvmlVgpuInstanceGetEncoderSessions` """ @@ -25672,10 +26749,12 @@ cpdef object vgpu_instance_get_fbc_stats(unsigned int vgpu_instance): """Retrieves the active frame buffer capture sessions statistics of a vGPU Instance. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: - nvmlFBCStats_t: Reference to ``nvmlFBCStats_t`` structure containing NvFBC stats. + nvmlFBCStats_t: Reference to ``nvmlFBCStats_t`` structure + containing NvFBC stats. .. seealso:: `nvmlVgpuInstanceGetFBCStats` """ @@ -25691,10 +26770,12 @@ cpdef object vgpu_instance_get_fbc_sessions(unsigned int vgpu_instance): """Retrieves information about active frame buffer capture sessions on a vGPU Instance. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: - nvmlFBCSessionInfo_t: Reference in which to return the session information. + nvmlFBCSessionInfo_t: Reference in which to return the session + information. .. seealso:: `nvmlVgpuInstanceGetFBCSessions` """ @@ -25716,7 +26797,8 @@ cpdef unsigned int vgpu_instance_get_gpu_instance_id(unsigned int vgpu_instance) """Retrieve the GPU Instance ID for the given vGPU Instance. The API will return a valid GPU Instance ID for MIG backed vGPU Instance, else INVALID_GPU_INSTANCE_ID is returned. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: unsigned int: GPU Instance ID. @@ -25734,7 +26816,8 @@ cpdef str vgpu_instance_get_gpu_pci_id(unsigned int vgpu_instance): """Retrieves the PCI Id of the given vGPU Instance i.e. the PCI Id of the GPU as seen inside the VM. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: char: Caller-supplied buffer to return vGPU PCI Id string. @@ -25760,10 +26843,12 @@ cpdef unsigned int vgpu_type_get_capabilities(unsigned int vgpu_type_id, int cap Args: vgpu_type_id (unsigned int): Handle to vGPU type. - capability (VgpuCapability): Specifies the ``nvmlVgpuCapability_t`` to be queried. + capability (VgpuCapability): Specifies the + ``nvmlVgpuCapability_t`` to be queried. Returns: - unsigned int: A boolean for the queried capability indicating that feature is supported. + unsigned int: A boolean for the queried capability indicating + that feature is supported. .. seealso:: `nvmlVgpuTypeGetCapabilities` """ @@ -25778,7 +26863,8 @@ cpdef str vgpu_instance_get_mdev_uuid(unsigned int vgpu_instance): """Retrieve the MDEV UUID of a vGPU instance. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: char: Pointer to caller-supplied buffer to hold MDEV UUID. @@ -25798,7 +26884,8 @@ cpdef gpu_instance_set_vgpu_scheduler_state(intptr_t gpu_instance, intptr_t p_sc Args: gpu_instance (intptr_t): The GPU instance handle. - p_scheduler (intptr_t): Pointer to the caller-provided structure of ``nvmlVgpuSchedulerState_t``. + p_scheduler (intptr_t): Pointer to the caller-provided + structure of ``nvmlVgpuSchedulerState_t``. .. seealso:: `nvmlGpuInstanceSetVgpuSchedulerState` """ @@ -25815,7 +26902,8 @@ cpdef object gpu_instance_get_vgpu_scheduler_state(intptr_t gpu_instance): gpu_instance (intptr_t): The GPU instance handle. Returns: - nvmlVgpuSchedulerStateInfo_v1_t: Reference in which ``p_scheduler_state_info`` is returned. + nvmlVgpuSchedulerStateInfo_v1_t: Reference in which + ``p_scheduler_state_info`` is returned. .. seealso:: `nvmlGpuInstanceGetVgpuSchedulerState` """ @@ -25835,7 +26923,8 @@ cpdef object gpu_instance_get_vgpu_scheduler_log(intptr_t gpu_instance): gpu_instance (intptr_t): The GPU instance handle. Returns: - nvmlVgpuSchedulerLogInfo_v1_t: Reference in which ``p_scheduler_log_info`` is written. + nvmlVgpuSchedulerLogInfo_v1_t: Reference in which + ``p_scheduler_log_info`` is written. .. seealso:: `nvmlGpuInstanceGetVgpuSchedulerLog` """ @@ -25855,7 +26944,8 @@ cpdef str device_get_pgpu_metadata_string(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - char: Pointer to caller-supplied buffer into which ``pgpu_metadata`` is written. + char: Pointer to caller-supplied buffer into which + ``pgpu_metadata`` is written. .. seealso:: `nvmlDeviceGetPgpuMetadataString` """ @@ -25880,7 +26970,8 @@ cpdef object device_get_vgpu_scheduler_log(intptr_t device): device (intptr_t): The identifier of the target ``device``. Returns: - nvmlVgpuSchedulerLog_t: Reference in which ``p_scheduler_log`` is written. + nvmlVgpuSchedulerLog_t: Reference in which ``p_scheduler_log`` + is written. .. seealso:: `nvmlDeviceGetVgpuSchedulerLog` """ @@ -25899,7 +26990,8 @@ cpdef object device_get_vgpu_scheduler_state(intptr_t device): device (intptr_t): The identifier of the target ``device``. Returns: - nvmlVgpuSchedulerGetState_t: Reference in which ``p_scheduler_state`` is returned. + nvmlVgpuSchedulerGetState_t: Reference in which + ``p_scheduler_state`` is returned. .. seealso:: `nvmlDeviceGetVgpuSchedulerState` """ @@ -25918,7 +27010,8 @@ cpdef object device_get_vgpu_scheduler_capabilities(intptr_t device): device (intptr_t): The identifier of the target ``device``. Returns: - nvmlVgpuSchedulerCapabilities_t: Reference in which ``p_capabilities`` is written. + nvmlVgpuSchedulerCapabilities_t: Reference in which + ``p_capabilities`` is written. .. seealso:: `nvmlDeviceGetVgpuSchedulerCapabilities` """ @@ -25935,7 +27028,8 @@ cpdef device_set_vgpu_scheduler_state(intptr_t device, intptr_t p_scheduler_stat Args: device (intptr_t): The identifier of the target ``device``. - p_scheduler_state (intptr_t): vGPU ``p_scheduler_state`` to set. + p_scheduler_state (intptr_t): vGPU ``p_scheduler_state`` to + set. .. seealso:: `nvmlDeviceSetVgpuSchedulerState` """ @@ -25948,7 +27042,8 @@ cpdef set_vgpu_version(intptr_t vgpu_version): """Override the preset range of vGPU versions supported by the NVIDIA vGPU Manager with a range set by an administrator. Args: - vgpu_version (intptr_t): Pointer to a caller-supplied range of supported vGPU versions. + vgpu_version (intptr_t): Pointer to a caller-supplied range of + supported vGPU versions. .. seealso:: `nvmlSetVgpuVersion` """ @@ -25962,13 +27057,17 @@ cpdef tuple device_get_vgpu_process_utilization(intptr_t device, unsigned long l Args: device (intptr_t): The identifier for the target device. - last_seen_time_stamp (unsigned long long): Return only samples with timestamp greater than last_seen_time_stamp. + last_seen_time_stamp (unsigned long long): Return only samples + with timestamp greater than last_seen_time_stamp. Returns: A 2-tuple containing: - - unsigned int: Pointer to caller-supplied array size, and returns number of processes running on vGPU instances. - - nvmlVgpuProcessUtilizationSample_t: Pointer to caller-supplied buffer in which vGPU sub process utilization samples are returned. + - unsigned int: Pointer to caller-supplied array size, and + returns number of processes running on vGPU instances. + - nvmlVgpuProcessUtilizationSample_t: Pointer to caller-supplied + buffer in which vGPU sub process utilization samples are + returned. .. seealso:: `nvmlDeviceGetVgpuProcessUtilization` """ @@ -25984,7 +27083,8 @@ cpdef int vgpu_instance_get_accounting_mode(unsigned int vgpu_instance) except? """Queries the state of per process accounting mode on vGPU. Args: - vgpu_instance (unsigned int): The identifier of the target vGPU instance. + vgpu_instance (unsigned int): The identifier of the target + vGPU instance. Returns: int: Reference in which to return the current accounting mode. @@ -26002,10 +27102,12 @@ cpdef object vgpu_instance_get_accounting_pids(unsigned int vgpu_instance): """Queries list of processes running on vGPU that can be queried for accounting stats. The list of processes returned can be in running or terminated state. Args: - vgpu_instance (unsigned int): The identifier of the target vGPU instance. + vgpu_instance (unsigned int): The identifier of the target + vGPU instance. Returns: - unsigned int: Reference in which to return list of process ids. + unsigned int: Reference in which to return list of process + ids. .. seealso:: `nvmlVgpuInstanceGetAccountingPids` """ @@ -26027,11 +27129,14 @@ cpdef object vgpu_instance_get_accounting_stats(unsigned int vgpu_instance, unsi """Queries process's accounting stats. Args: - vgpu_instance (unsigned int): The identifier of the target vGPU instance. - pid (unsigned int): Process Id of the target process to query stats for. + vgpu_instance (unsigned int): The identifier of the target + vGPU instance. + pid (unsigned int): Process Id of the target process to query + stats for. Returns: - nvmlAccountingStats_t: Reference in which to return the process's accounting stats. + nvmlAccountingStats_t: Reference in which to return the + process's accounting stats. .. seealso:: `nvmlVgpuInstanceGetAccountingStats` """ @@ -26047,7 +27152,8 @@ cpdef vgpu_instance_clear_accounting_pids(unsigned int vgpu_instance): """Clears accounting information of the vGPU instance that have already terminated. Args: - vgpu_instance (unsigned int): The identifier of the target vGPU instance. + vgpu_instance (unsigned int): The identifier of the target + vGPU instance. .. seealso:: `nvmlVgpuInstanceClearAccountingPids` """ @@ -26060,10 +27166,12 @@ cpdef object vgpu_instance_get_license_info_v2(unsigned int vgpu_instance): """Query the license information of the vGPU instance. Args: - vgpu_instance (unsigned int): Identifier of the target vGPU instance. + vgpu_instance (unsigned int): Identifier of the target vGPU + instance. Returns: - nvmlVgpuLicenseInfo_t: Pointer to vGPU license information structure. + nvmlVgpuLicenseInfo_t: Pointer to vGPU license information + structure. .. seealso:: `nvmlVgpuInstanceGetLicenseInfo_v2` """ @@ -26079,7 +27187,8 @@ cpdef unsigned int get_excluded_device_count() except? 0: """Retrieves the number of excluded GPU devices in the system. Returns: - unsigned int: Reference in which to return the number of excluded devices. + unsigned int: Reference in which to return the number of + excluded devices. .. seealso:: `nvmlGetExcludedDeviceCount` """ @@ -26094,10 +27203,12 @@ cpdef object get_excluded_device_info_by_index(unsigned int index): """Acquire the device information for an excluded GPU device, based on its index. Args: - index (unsigned int): The index of the target GPU, >= 0 and < ``deviceCount``. + index (unsigned int): The index of the target GPU, >= 0 and < + ``deviceCount``. Returns: - nvmlExcludedDeviceInfo_t: Reference in which to return the device information. + nvmlExcludedDeviceInfo_t: Reference in which to return the + device information. .. seealso:: `nvmlGetExcludedDeviceInfoByIndex` """ @@ -26114,7 +27225,8 @@ cpdef int device_set_mig_mode(intptr_t device, unsigned int mode) except? -1: Args: device (intptr_t): The identifier of the target device. - mode (unsigned int): The mode to be set, ``NVML_DEVICE_MIG_DISABLE`` or ``NVML_DEVICE_MIG_ENABLE``. + mode (unsigned int): The mode to be set, + ``NVML_DEVICE_MIG_DISABLE`` or ``NVML_DEVICE_MIG_ENABLE``. Returns: int: The activation_status status. @@ -26137,8 +27249,10 @@ cpdef tuple device_get_mig_mode(intptr_t device): Returns: A 2-tuple containing: - - unsigned int: Returns the current mode, ``NVML_DEVICE_MIG_DISABLE`` or ``NVML_DEVICE_MIG_ENABLE``. - - unsigned int: Returns the pending mode, ``NVML_DEVICE_MIG_DISABLE`` or ``NVML_DEVICE_MIG_ENABLE``. + - unsigned int: Returns the current mode, + ``NVML_DEVICE_MIG_DISABLE`` or ``NVML_DEVICE_MIG_ENABLE``. + - unsigned int: Returns the pending mode, + ``NVML_DEVICE_MIG_DISABLE`` or ``NVML_DEVICE_MIG_ENABLE``. .. seealso:: `nvmlDeviceGetMigMode` """ @@ -26155,10 +27269,15 @@ cpdef object device_get_gpu_instance_possible_placements_v2(intptr_t device, uns Args: device (intptr_t): The identifier of the target device. - profile_id (unsigned int): The GPU instance profile ID. See ``nvmlDeviceGetGpuInstanceProfileInfo``. + profile_id (unsigned int): The GPU instance profile ID. See + ``nvmlDeviceGetGpuInstanceProfileInfo``. Returns: - nvmlGpuInstancePlacement_t: Returns placements allowed for the profile. Can be NULL to discover number of allowed placements for this profile. If non-NULL must be large enough to accommodate the placements supported by the profile. + nvmlGpuInstancePlacement_t: Returns placements allowed for the + profile. Can be NULL to discover number of allowed + placements for this profile. If non-NULL must be large + enough to accommodate the placements supported by the + profile. .. seealso:: `nvmlDeviceGetGpuInstancePossiblePlacements_v2` """ @@ -26181,10 +27300,12 @@ cpdef unsigned int device_get_gpu_instance_remaining_capacity(intptr_t device, u Args: device (intptr_t): The identifier of the target device. - profile_id (unsigned int): The GPU instance profile ID. See ``nvmlDeviceGetGpuInstanceProfileInfo``. + profile_id (unsigned int): The GPU instance profile ID. See + ``nvmlDeviceGetGpuInstanceProfileInfo``. Returns: - unsigned int: Returns remaining instance count for the profile ID. + unsigned int: Returns remaining instance count for the profile + ID. .. seealso:: `nvmlDeviceGetGpuInstanceRemainingCapacity` """ @@ -26200,7 +27321,8 @@ cpdef intptr_t device_create_gpu_instance(intptr_t device, unsigned int profile_ Args: device (intptr_t): The identifier of the target device. - profile_id (unsigned int): The GPU instance profile ID. See ``nvmlDeviceGetGpuInstanceProfileInfo``. + profile_id (unsigned int): The GPU instance profile ID. See + ``nvmlDeviceGetGpuInstanceProfileInfo``. Returns: intptr_t: Returns the GPU instance handle. @@ -26219,8 +27341,10 @@ cpdef intptr_t device_create_gpu_instance_with_placement(intptr_t device, unsign Args: device (intptr_t): The identifier of the target device. - profile_id (unsigned int): The GPU instance profile ID. See ``nvmlDeviceGetGpuInstanceProfileInfo``. - placement (intptr_t): The requested placement. See ``nvmlDeviceGetGpuInstancePossiblePlacements_v2``. + profile_id (unsigned int): The GPU instance profile ID. See + ``nvmlDeviceGetGpuInstanceProfileInfo``. + placement (intptr_t): The requested placement. See + ``nvmlDeviceGetGpuInstancePossiblePlacements_v2``. Returns: intptr_t: Returns the GPU instance handle. @@ -26289,12 +27413,16 @@ cpdef object gpu_instance_get_compute_instance_profile_info_v(intptr_t gpu_insta """Versioned wrapper around ``nvmlGpuInstanceGetComputeInstanceProfileInfo`` that accepts a versioned ``nvmlComputeInstanceProfileInfo_v2_t`` or later output structure. Args: - gpu_instance (intptr_t): The identifier of the target GPU instance. - profile (unsigned int): One of the NVML_COMPUTE_INSTANCE_PROFILE_*. - eng_profile (unsigned int): One of the NVML_COMPUTE_INSTANCE_ENGINE_PROFILE_*. + gpu_instance (intptr_t): The identifier of the target GPU + instance. + profile (unsigned int): One of the + NVML_COMPUTE_INSTANCE_PROFILE_*. + eng_profile (unsigned int): One of the + NVML_COMPUTE_INSTANCE_ENGINE_PROFILE_*. Returns: - nvmlComputeInstanceProfileInfo_v2_t: Returns detailed profile information. + nvmlComputeInstanceProfileInfo_v2_t: Returns detailed profile + information. .. seealso:: `nvmlGpuInstanceGetComputeInstanceProfileInfoV` """ @@ -26311,11 +27439,14 @@ cpdef unsigned int gpu_instance_get_compute_instance_remaining_capacity(intptr_t """Get compute instance profile capacity. Args: - gpu_instance (intptr_t): The identifier of the target GPU instance. - profile_id (unsigned int): The compute instance profile ID. See ``nvmlGpuInstanceGetComputeInstanceProfileInfo``. + gpu_instance (intptr_t): The identifier of the target GPU + instance. + profile_id (unsigned int): The compute instance profile ID. + See ``nvmlGpuInstanceGetComputeInstanceProfileInfo``. Returns: - unsigned int: Returns remaining instance count for the profile ID. + unsigned int: Returns remaining instance count for the profile + ID. .. seealso:: `nvmlGpuInstanceGetComputeInstanceRemainingCapacity` """ @@ -26330,11 +27461,17 @@ cpdef object gpu_instance_get_compute_instance_possible_placements(intptr_t gpu_ """Get compute instance placements. Args: - gpu_instance (intptr_t): The identifier of the target GPU instance. - profile_id (unsigned int): The compute instance profile ID. See ``nvmlGpuInstanceGetComputeInstanceProfileInfo``. + gpu_instance (intptr_t): The identifier of the target GPU + instance. + profile_id (unsigned int): The compute instance profile ID. + See ``nvmlGpuInstanceGetComputeInstanceProfileInfo``. Returns: - nvmlComputeInstancePlacement_t: Returns placements allowed for the profile. Can be NULL to discover number of allowed placements for this profile. If non-NULL must be large enough to accommodate the placements supported by the profile. + nvmlComputeInstancePlacement_t: Returns placements allowed for + the profile. Can be NULL to discover number of allowed + placements for this profile. If non-NULL must be large + enough to accommodate the placements supported by the + profile. .. seealso:: `nvmlGpuInstanceGetComputeInstancePossiblePlacements` """ @@ -26356,8 +27493,10 @@ cpdef intptr_t gpu_instance_create_compute_instance(intptr_t gpu_instance, unsig """Create compute instance. Args: - gpu_instance (intptr_t): The identifier of the target GPU instance. - profile_id (unsigned int): The compute instance profile ID. See ``nvmlGpuInstanceGetComputeInstanceProfileInfo``. + gpu_instance (intptr_t): The identifier of the target GPU + instance. + profile_id (unsigned int): The compute instance profile ID. + See ``nvmlGpuInstanceGetComputeInstanceProfileInfo``. Returns: intptr_t: Returns the compute instance handle. @@ -26375,9 +27514,12 @@ cpdef intptr_t gpu_instance_create_compute_instance_with_placement(intptr_t gpu_ """Create compute instance with the specified placement. Args: - gpu_instance (intptr_t): The identifier of the target GPU instance. - profile_id (unsigned int): The compute instance profile ID. See ``nvmlGpuInstanceGetComputeInstanceProfileInfo``. - placement (intptr_t): The requested placement. See ``nvmlGpuInstanceGetComputeInstancePossiblePlacements``. + gpu_instance (intptr_t): The identifier of the target GPU + instance. + profile_id (unsigned int): The compute instance profile ID. + See ``nvmlGpuInstanceGetComputeInstanceProfileInfo``. + placement (intptr_t): The requested placement. See + ``nvmlGpuInstanceGetComputeInstancePossiblePlacements``. Returns: intptr_t: Returns the compute instance handle. @@ -26408,7 +27550,8 @@ cpdef intptr_t gpu_instance_get_compute_instance_by_id(intptr_t gpu_instance, un """Get compute instance for given instance ID. Args: - gpu_instance (intptr_t): The identifier of the target GPU instance. + gpu_instance (intptr_t): The identifier of the target GPU + instance. id (unsigned int): The compute instance ID. Returns: @@ -26430,7 +27573,8 @@ cpdef object compute_instance_get_info_v2(intptr_t compute_instance): compute_instance (intptr_t): The compute instance handle. Returns: - nvmlComputeInstanceInfo_t: Return compute instance information. + nvmlComputeInstanceInfo_t: Return compute instance + information. .. seealso:: `nvmlComputeInstanceGetInfo_v2` """ @@ -26556,7 +27700,10 @@ cpdef device_power_smoothing_activate_preset_profile(intptr_t device, intptr_t p Args: device (intptr_t): The identifier of the target device. - profile (intptr_t): Reference to ``nvmlPowerSmoothingProfile_v1_t``. Note that only ``profile->profileId`` is used and the rest of the structure is ignored. + profile (intptr_t): Reference to + ``nvmlPowerSmoothingProfile_v1_t``. Note that only + ``profile->profileId`` is used and the rest of the + structure is ignored. .. seealso:: `nvmlDevicePowerSmoothingActivatePresetProfile` """ @@ -26570,7 +27717,8 @@ cpdef device_power_smoothing_update_preset_profile_param(intptr_t device, intptr Args: device (intptr_t): The identifier of the target device. - profile (intptr_t): Reference to ``nvmlPowerSmoothingProfile_v1_t`` struct. + profile (intptr_t): Reference to + ``nvmlPowerSmoothingProfile_v1_t`` struct. .. seealso:: `nvmlDevicePowerSmoothingUpdatePresetProfileParam` """ @@ -26584,7 +27732,8 @@ cpdef device_power_smoothing_set_state(intptr_t device, intptr_t state): Args: device (intptr_t): The identifier of the target device. - state (intptr_t): Reference to ``nvmlPowerSmoothingState_v1_t``. + state (intptr_t): Reference to + ``nvmlPowerSmoothingState_v1_t``. .. seealso:: `nvmlDevicePowerSmoothingSetState` """ @@ -26600,7 +27749,8 @@ cpdef object device_get_addressing_mode(intptr_t device): device (intptr_t): The device handle. Returns: - nvmlDeviceAddressingMode_v1_t: Pointer to addressing mode of the device. + nvmlDeviceAddressingMode_v1_t: Pointer to addressing mode of + the device. .. seealso:: `nvmlDeviceGetAddressingMode` """ @@ -26640,7 +27790,8 @@ cpdef object device_get_power_mizer_mode_v1(intptr_t device): device (intptr_t): The identifier of the target device. Returns: - nvmlDevicePowerMizerModes_v1_t: Reference in which to return the power mizer mode. + nvmlDevicePowerMizerModes_v1_t: Reference in which to return + the power mizer mode. .. seealso:: `nvmlDeviceGetPowerMizerMode_v1` """ @@ -26657,7 +27808,8 @@ cpdef device_set_power_mizer_mode_v1(intptr_t device, intptr_t power_mizer_mode) Args: device (intptr_t): The identifier of the target device. - power_mizer_mode (intptr_t): Reference in which to set the power mizer mode. + power_mizer_mode (intptr_t): Reference in which to set the + power mizer mode. .. seealso:: `nvmlDeviceSetPowerMizerMode_v1` """ @@ -26686,7 +27838,8 @@ cpdef object device_get_vgpu_scheduler_state_v2(intptr_t device): device (intptr_t): The identifier of the target ``device``. Returns: - nvmlVgpuSchedulerStateInfo_v2_t: Reference in which ``p_scheduler_state_info`` is returned. + nvmlVgpuSchedulerStateInfo_v2_t: Reference in which + ``p_scheduler_state_info`` is returned. .. seealso:: `nvmlDeviceGetVgpuSchedulerState_v2` """ @@ -26705,7 +27858,8 @@ cpdef object gpu_instance_get_vgpu_scheduler_state_v2(intptr_t gpu_instance): gpu_instance (intptr_t): The GPU instance handle. Returns: - nvmlVgpuSchedulerStateInfo_v2_t: Reference in which ``p_scheduler_state_info`` is returned. + nvmlVgpuSchedulerStateInfo_v2_t: Reference in which + ``p_scheduler_state_info`` is returned. .. seealso:: `nvmlGpuInstanceGetVgpuSchedulerState_v2` """ @@ -26724,7 +27878,8 @@ cpdef object device_get_vgpu_scheduler_log_v2(intptr_t device): device (intptr_t): The identifier of the target ``device``. Returns: - nvmlVgpuSchedulerLogInfo_v2_t: Reference in which ``p_scheduler_log_info`` is written. + nvmlVgpuSchedulerLogInfo_v2_t: Reference in which + ``p_scheduler_log_info`` is written. .. seealso:: `nvmlDeviceGetVgpuSchedulerLog_v2` """ @@ -26743,7 +27898,8 @@ cpdef object gpu_instance_get_vgpu_scheduler_log_v2(intptr_t gpu_instance): gpu_instance (intptr_t): The GPU instance handle. Returns: - nvmlVgpuSchedulerLogInfo_v2_t: Reference in which ``p_scheduler_log_info`` is written. + nvmlVgpuSchedulerLogInfo_v2_t: Reference in which + ``p_scheduler_log_info`` is written. .. seealso:: `nvmlGpuInstanceGetVgpuSchedulerLog_v2` """ @@ -26760,7 +27916,8 @@ cpdef device_set_vgpu_scheduler_state_v2(intptr_t device, intptr_t p_scheduler_s Args: device (intptr_t): The identifier of the target ``device``. - p_scheduler_state (intptr_t): vGPU ``p_scheduler_state`` to set. + p_scheduler_state (intptr_t): vGPU ``p_scheduler_state`` to + set. .. seealso:: `nvmlDeviceSetVgpuSchedulerState_v2` """ @@ -26774,7 +27931,8 @@ cpdef gpu_instance_set_vgpu_scheduler_state_v2(intptr_t gpu_instance, intptr_t p Args: gpu_instance (intptr_t): The GPU instance handle. - p_scheduler_state (intptr_t): Pointer to the caller-provided structure of ``nvmlVgpuSchedulerState_v2_t``. + p_scheduler_state (intptr_t): Pointer to the caller-provided + structure of ``nvmlVgpuSchedulerState_v2_t``. .. seealso:: `nvmlGpuInstanceSetVgpuSchedulerState_v2` """ @@ -26783,6 +27941,88 @@ cpdef gpu_instance_set_vgpu_scheduler_state_v2(intptr_t gpu_instance, intptr_t p check_status(__status__) +cpdef object system_get_cper_v1(): + """Retrieves Common Platform Error Record (CPER) data. + + Returns: + nvmlGetCPER_v1_t: Pointer to an ``nvmlGetCPER_v1_t``. On entry + set ``cursor.cperTypeMask``, ``cursor.uuid`` (empty string + for all), ``cursor.handle`` (to + ``NVML_CPER_CURSOR_HANDLE_INIT`` for first call), + ``buffer`` (or NULL), ``bufferSize``. On return + ``cursor.handle`` and ``bufferSize`` are updated. + + .. seealso:: `nvmlSystemGetCPER_v1` + """ + cdef GetCPER_v1 cper_py = GetCPER_v1() + cdef nvmlGetCPER_v1_t *cper = (cper_py._get_ptr()) + with nogil: + __status__ = nvmlSystemGetCPER_v1(cper) + check_status(__status__) + return cper_py + + +cpdef object device_get_bbx_time_data_v1(intptr_t device): + """Retrieves the cumulative number of seconds the GPU has had the driver loaded. + + Args: + device (intptr_t): The identifier of the target device. + + Returns: + nvmlBBXTimeData_v1_t: Reference in which to return the + cumulative number of seconds the GPU has had the driver + loaded. + + .. seealso:: `nvmlDeviceGetBBXTimeData_v1` + """ + cdef BBXTimeData_v1 time_data_py = BBXTimeData_v1() + cdef nvmlBBXTimeData_v1_t *time_data = (time_data_py._get_ptr()) + with nogil: + __status__ = nvmlDeviceGetBBXTimeData_v1(device, time_data) + check_status(__status__) + return time_data_py + + +cpdef object device_get_accounting_stats_v2(intptr_t device): + """Queries process's accounting stats (v2). + + Args: + device (intptr_t): The identifier of the target device. + + Returns: + nvmlAccountingStats_v2_t: Reference in which to return the + process's accounting stats (v2). + + .. seealso:: `nvmlDeviceGetAccountingStats_v2` + """ + cdef AccountingStats_v2 stats_py = AccountingStats_v2() + cdef nvmlAccountingStats_v2_t *stats = (stats_py._get_ptr()) + with nogil: + __status__ = nvmlDeviceGetAccountingStats_v2(device, stats) + check_status(__status__) + return stats_py + + +cpdef object device_get_remapped_rows_v2(intptr_t device): + """Get the status of row remapper. + + Args: + device (intptr_t): The identifier of the target device. + + Returns: + nvmlRemappedRowsInfo_v2_t: Reference for + ``nvmlRemappedRowsInfo_v2_t``. + + .. seealso:: `nvmlDeviceGetRemappedRows_v2` + """ + cdef RemappedRowsInfo_v2 info_py = RemappedRowsInfo_v2() + cdef nvmlRemappedRowsInfo_v2_t *info = (info_py._get_ptr()) + with nogil: + __status__ = nvmlDeviceGetRemappedRows_v2(device, info) + check_status(__status__) + return info_py + + cpdef object system_get_topology_gpu_set(unsigned int cpuNumber): """Retrieve the set of GPUs that have a CPU affinity with the given CPU number @@ -28466,8 +29706,5 @@ cpdef str vgpu_type_get_name(unsigned int vgpu_type_id): return cpython.PyUnicode_FromStringAndSize(vgpu_type_name, size[0]) -# Cleanup some docstrings that don't parse as rst. -device_get_virtualization_mode.__doc__ = device_get_virtualization_mode.__doc__.replace("NVML_GPU_VIRTUALIZATION_?", "``NVML_GPU_VIRTUALIZATION_?``") -device_set_virtualization_mode.__doc__ = device_set_virtualization_mode.__doc__.replace("NVML_GPU_VIRTUALIZATION_?", "``NVML_GPU_VIRTUALIZATION_?``") -GpmMetricId.GPM_METRIC_DRAM_BW_UTIL.__doc__ = "Percentage of DRAM bw used vs theoretical maximum. ``0.0 - 100.0 *\u200d/``." + del _cyb_FastEnum diff --git a/cuda_bindings/cuda/bindings/nvvm.pyx b/cuda_bindings/cuda/bindings/nvvm.pyx index 6d18a50f24c..abbbd4a72bd 100644 --- a/cuda_bindings/cuda/bindings/nvvm.pyx +++ b/cuda_bindings/cuda/bindings/nvvm.pyx @@ -3,7 +3,7 @@ # SPDX-License-Identifier: Apache-2.0 # # This code was automatically generated across versions from 12.0.1 to 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=82dc56ccc695031faa515d1971c9841131d5aadc60c6d6e6cc223580fc544d16 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=869e6761e7af952be9590fcd26675047c19ff23ee9c1521f64dd7e8f6842bced # <<<< PREAMBLE CONTENT >>>> @@ -162,9 +162,11 @@ cpdef add_module_to_program(intptr_t prog, buffer, size_t size, name): Args: prog (intptr_t): NVVM program. - buffer (bytes): NVVM IR module in the bitcode or text representation. + buffer (bytes): NVVM IR module in the bitcode or text + representation. size (size_t): Size of the NVVM IR module. - name (str): Name of the NVVM IR module. If NULL, "" is used as the name. + name (str): Name of the NVVM IR module. If NULL, "" + is used as the name. .. seealso:: `nvvmAddModuleToProgram` """ @@ -185,7 +187,8 @@ cpdef lazy_add_module_to_program(intptr_t prog, buffer, size_t size, name): prog (intptr_t): NVVM program. buffer (bytes): NVVM IR module in the bitcode representation. size (size_t): Size of the NVVM IR module. - name (str): Name of the NVVM IR module. If NULL, "" is used as the name. + name (str): Name of the NVVM IR module. If NULL, "" + is used as the name. .. seealso:: `nvvmLazyAddModuleToProgram` """ @@ -205,7 +208,8 @@ cpdef compile_program(intptr_t prog, int num_options, options): Args: prog (intptr_t): NVVM program. num_options (int): Number of compiler ``options`` passed. - options (object): Compiler options in the form of C string array. It can be: + options (object): Compiler options in the form of C string + array. It can be: - an :class:`int` as the pointer address to the nested sequence, or - a Python sequence of :class:`int`\s, each of which is a pointer address @@ -228,7 +232,8 @@ cpdef verify_program(intptr_t prog, int num_options, options): Args: prog (intptr_t): NVVM program. num_options (int): Number of compiler ``options`` passed. - options (object): Compiler options in the form of C string array. It can be: + options (object): Compiler options in the form of C string + array. It can be: - an :class:`int` as the pointer address to the nested sequence, or - a Python sequence of :class:`int`\s, each of which is a pointer address @@ -252,7 +257,8 @@ cpdef size_t get_compiled_result_size(intptr_t prog) except? 0: prog (intptr_t): NVVM program. Returns: - size_t: Size of the compiled result (including the trailing NULL). + size_t: Size of the compiled result (including the trailing + NULL). .. seealso:: `nvvmGetCompiledResultSize` """ @@ -285,7 +291,8 @@ cpdef size_t get_program_log_size(intptr_t prog) except? 0: prog (intptr_t): NVVM program. Returns: - size_t: Size of the compilation/verification log (including the trailing NULL). + size_t: Size of the compilation/verification log (including + the trailing NULL). .. seealso:: `nvvmGetProgramLogSize` """ diff --git a/cuda_bindings/cuda/bindings/runtime.pxd b/cuda_bindings/cuda/bindings/runtime.pxd index 7cb680d1743..39e2d129890 100644 --- a/cuda_bindings/cuda/bindings/runtime.pxd +++ b/cuda_bindings/cuda/bindings/runtime.pxd @@ -2,7 +2,7 @@ # SPDX-License-Identifier: Apache-2.0 # This code was automatically generated with version 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=0f2431380680008795336b7acb5ccd83dba7a6e05d0c81c2b5f825bc95576ccd +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=033835aa1fcce7bcd75db8c655b92a6415a74fe0734819cda666ebf038bc1bce cimport cuda.bindings.cyruntime as cyruntime include "_lib/utils.pxd" @@ -405,10 +405,6 @@ cdef class cudaArraySparseProperties: Flags will either be zero or cudaArraySparsePropertiesSingleMipTail - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -435,10 +431,6 @@ cdef class cudaArrayMemoryRequirements: Alignment necessary for mapping the array. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -615,10 +607,6 @@ cdef class cudaMemcpyNodeParams: Must be zero - reserved : int - Must be zero - - ctx : cudaExecutionContext_t Context in which to run the memcpy. If NULL will try to use the current context. @@ -1025,13 +1013,6 @@ cdef class anon_struct4: cdef class anon_struct5: """ - Attributes - ---------- - - reserved : list[int] - - - Methods ------- getPtr() @@ -1060,10 +1041,6 @@ cdef class anon_union0: - reserved : anon_struct5 - - - Methods ------- getPtr() @@ -1083,9 +1060,6 @@ cdef class anon_union0: cdef anon_struct4 _pitch2D - cdef anon_struct5 _reserved - - cdef class cudaResourceDesc: """ CUDA resource descriptor @@ -1155,10 +1129,6 @@ cdef class cudaResourceViewDesc: Last layer index - reserved : list[unsigned int] - Must be zero - - Methods ------- getPtr() @@ -1201,10 +1171,6 @@ cdef class cudaPointerAttributes: pointer if an invalid pointer has been passed to CUDA. - reserved : list[long] - Must be zero - - Methods ------- getPtr() @@ -1333,14 +1299,6 @@ cdef class cudaFuncAttributes: the value. - reserved1 : int - - - - reserved : list[int] - Reserved for future use. - - Methods ------- getPtr() @@ -1440,10 +1398,6 @@ cdef class cudaMemPoolProps: Bitmask indicating intended usage for the pool. - reserved : bytes - reserved for future use, must be 0 - - Methods ------- getPtr() @@ -1462,13 +1416,6 @@ cdef class cudaMemPoolPtrExportData: """ Opaque data for exporting a pool allocation - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -2236,10 +2183,6 @@ cdef class cudaDeviceProp: multi-node system. - reserved : list[int] - Reserved for future use - - Methods ------- getPtr() @@ -2255,13 +2198,6 @@ cdef class cudaIpcEventHandle_st: """ CUDA IPC event handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -2274,13 +2210,6 @@ cdef class cudaIpcMemHandle_st: """ CUDA IPC memory handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -2291,13 +2220,6 @@ cdef class cudaIpcMemHandle_st: cdef class cudaMemFabricHandle_st: """ - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -2385,10 +2307,6 @@ cdef class cudaExternalMemoryHandleDesc: Flags must either be zero or cudaExternalMemoryDedicated - reserved : list[unsigned int] - Must be zero - - Methods ------- getPtr() @@ -2419,10 +2337,6 @@ cdef class cudaExternalMemoryBufferDesc: Flags reserved for future use. Must be zero. - reserved : list[unsigned int] - Must be zero - - Methods ------- getPtr() @@ -2460,10 +2374,6 @@ cdef class cudaExternalMemoryMipmappedArrayDesc: Total number of levels in the mipmap chain - reserved : list[unsigned int] - Must be zero - - Methods ------- getPtr() @@ -2553,10 +2463,6 @@ cdef class cudaExternalSemaphoreHandleDesc: Flags reserved for the future. Must be zero. - reserved : list[unsigned int] - Must be zero - - Methods ------- getPtr() @@ -2593,10 +2499,6 @@ cdef class anon_union5: - reserved : unsigned long long - - - Methods ------- getPtr() @@ -2640,10 +2542,6 @@ cdef class anon_struct12: - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -2682,10 +2580,6 @@ cdef class cudaExternalSemaphoreSignalParams: all other types of cudaExternalSemaphore_t, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -2722,10 +2616,6 @@ cdef class anon_union6: - reserved : unsigned long long - - - Methods ------- getPtr() @@ -2773,10 +2663,6 @@ cdef class anon_struct15: - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -2815,10 +2701,6 @@ cdef class cudaExternalSemaphoreWaitParams: all other types of cudaExternalSemaphore_t, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -2898,13 +2780,6 @@ cdef class cudaDevWorkqueueResource: """ Handle to a pre-existing workqueue related resource - Attributes - ---------- - - reserved : bytes - Reserved for future use - - Methods ------- getPtr() @@ -2939,10 +2814,6 @@ cdef class cudaDevSmResourceGroupParams_st: this this group is created. - reserved : list[unsigned int] - Reserved for future use - ensure this is zero initialized. - - Methods ------- getPtr() @@ -3477,14 +3348,6 @@ cdef class cudaGraphNodeParams: Type of the node - reserved0 : list[int] - Reserved. Must be zero. - - - reserved1 : list[long long] - Padding. Unused bytes must be zero. - - kernel : cudaKernelNodeParamsV2 Kernel node parameters. @@ -3533,10 +3396,6 @@ cdef class cudaGraphNodeParams: Conditional node parameters. - reserved2 : long long - Reserved bytes. Must be zero. - - Methods ------- getPtr() @@ -3618,11 +3477,6 @@ cdef class cudaGraphEdgeData_st: See cudaGraphDependencyType. - reserved : bytes - These bytes are unused and must be zeroed. This ensures - compatibility if additional fields are added in the future. - - Methods ------- getPtr() @@ -4023,12 +3877,12 @@ cdef class cudaLaunchAttributeValue: with the following fields: - `x` - The X dimension of the preferred cluster, in blocks. Must be a divisor of the grid X dimension, and must be a multiple of the `x` field of - ::cudaLaunchAttributeValue::clusterDim. - `y` - The Y dimension - of the preferred cluster, in blocks. Must be a divisor of the grid - Y dimension, and must be a multiple of the `y` field of - ::cudaLaunchAttributeValue::clusterDim. - `z` - The Z dimension - of the preferred cluster, in blocks. Must be equal to the `z` field - of ::cudaLaunchAttributeValue::clusterDim. + cudaLaunchAttributeValue::clusterDim. - `y` - The Y dimension of + the preferred cluster, in blocks. Must be a divisor of the grid Y + dimension, and must be a multiple of the `y` field of + cudaLaunchAttributeValue::clusterDim. - `z` - The Z dimension of + the preferred cluster, in blocks. Must be equal to the `z` field of + cudaLaunchAttributeValue::clusterDim. launchCompletionEvent : anon_struct20 @@ -4314,10 +4168,6 @@ cdef class cudaEglPlaneDesc_st: Channel Format Descriptor - reserved : list[unsigned int] - Reserved for future use - - Methods ------- getPtr() @@ -4430,13 +4280,6 @@ cdef class cudaIpcEventHandle_t(cudaIpcEventHandle_st): """ CUDA IPC event handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -4448,13 +4291,6 @@ cdef class cudaIpcMemHandle_t(cudaIpcMemHandle_st): """ CUDA IPC memory handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -4464,13 +4300,6 @@ cdef class cudaIpcMemHandle_t(cudaIpcMemHandle_st): cdef class cudaMemFabricHandle_t(cudaMemFabricHandle_st): """ - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -4504,10 +4333,6 @@ cdef class cudaDevSmResourceGroupParams(cudaDevSmResourceGroupParams_st): this this group is created. - reserved : list[unsigned int] - Reserved for future use - ensure this is zero initialized. - - Methods ------- getPtr() @@ -4609,11 +4434,6 @@ cdef class cudaGraphEdgeData(cudaGraphEdgeData_st): See cudaGraphDependencyType. - reserved : bytes - These bytes are unused and must be zeroed. This ensures - compatibility if additional fields are added in the future. - - Methods ------- getPtr() @@ -4830,12 +4650,12 @@ cdef class cudaStreamAttrValue(cudaLaunchAttributeValue): with the following fields: - `x` - The X dimension of the preferred cluster, in blocks. Must be a divisor of the grid X dimension, and must be a multiple of the `x` field of - ::cudaLaunchAttributeValue::clusterDim. - `y` - The Y dimension - of the preferred cluster, in blocks. Must be a divisor of the grid - Y dimension, and must be a multiple of the `y` field of - ::cudaLaunchAttributeValue::clusterDim. - `z` - The Z dimension - of the preferred cluster, in blocks. Must be equal to the `z` field - of ::cudaLaunchAttributeValue::clusterDim. + cudaLaunchAttributeValue::clusterDim. - `y` - The Y dimension of + the preferred cluster, in blocks. Must be a divisor of the grid Y + dimension, and must be a multiple of the `y` field of + cudaLaunchAttributeValue::clusterDim. - `z` - The Z dimension of + the preferred cluster, in blocks. Must be equal to the `z` field of + cudaLaunchAttributeValue::clusterDim. launchCompletionEvent : anon_struct20 @@ -4959,12 +4779,12 @@ cdef class cudaKernelNodeAttrValue(cudaLaunchAttributeValue): with the following fields: - `x` - The X dimension of the preferred cluster, in blocks. Must be a divisor of the grid X dimension, and must be a multiple of the `x` field of - ::cudaLaunchAttributeValue::clusterDim. - `y` - The Y dimension - of the preferred cluster, in blocks. Must be a divisor of the grid - Y dimension, and must be a multiple of the `y` field of - ::cudaLaunchAttributeValue::clusterDim. - `z` - The Z dimension - of the preferred cluster, in blocks. Must be equal to the `z` field - of ::cudaLaunchAttributeValue::clusterDim. + cudaLaunchAttributeValue::clusterDim. - `y` - The Y dimension of + the preferred cluster, in blocks. Must be a divisor of the grid Y + dimension, and must be a multiple of the `y` field of + cudaLaunchAttributeValue::clusterDim. - `z` - The Z dimension of + the preferred cluster, in blocks. Must be equal to the `z` field of + cudaLaunchAttributeValue::clusterDim. launchCompletionEvent : anon_struct20 @@ -5043,10 +4863,6 @@ cdef class cudaEglPlaneDesc(cudaEglPlaneDesc_st): Channel Format Descriptor - reserved : list[unsigned int] - Reserved for future use - - Methods ------- getPtr() diff --git a/cuda_bindings/cuda/bindings/runtime.pyx b/cuda_bindings/cuda/bindings/runtime.pyx index 6e11bdfc932..68359118522 100644 --- a/cuda_bindings/cuda/bindings/runtime.pyx +++ b/cuda_bindings/cuda/bindings/runtime.pyx @@ -2,7 +2,7 @@ # SPDX-License-Identifier: Apache-2.0 # This code was automatically generated with version 13.3.0. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=783d27cfa66fa4f5818edcf88141aeb96dcc0e27e73a77a36571f82f30f3bb47 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=aa972ab50217de282b9b3e566c903bc336a711bbef8cfe33c22d9dc6dc3f49d3 from typing import Any, Optional import cython import ctypes @@ -1748,8 +1748,8 @@ class cudaLaunchAttributeID(_FastEnum): cyruntime.cudaLaunchAttributeID.cudaLaunchAttributeDeviceUpdatableKernelNode, 'Valid for graph nodes, launches. This attribute is graphs-only, and passing\n' 'it to a launch in a non-capturing stream will result in an error.\n' - ' :cudaLaunchAttributeValue::deviceUpdatableKernelNode::deviceUpdatable can\n' - 'only be set to 0 or 1. Setting the field to 1 indicates that the\n' + ':py:obj:`~.cudaLaunchAttributeValue.deviceUpdatableKernelNode.deviceUpdatable`\n' + 'can only be set to 0 or 1. Setting the field to 1 indicates that the\n' 'corresponding kernel node should be device-updatable. On success, a handle\n' 'will be returned via\n' ':py:obj:`~.cudaLaunchAttributeValue.deviceUpdatableKernelNode.devNode`\n' @@ -6590,8 +6590,8 @@ class cudaStreamAttrID(_FastEnum): cyruntime.cudaLaunchAttributeID.cudaLaunchAttributeDeviceUpdatableKernelNode, 'Valid for graph nodes, launches. This attribute is graphs-only, and passing\n' 'it to a launch in a non-capturing stream will result in an error.\n' - ' :cudaLaunchAttributeValue::deviceUpdatableKernelNode::deviceUpdatable can\n' - 'only be set to 0 or 1. Setting the field to 1 indicates that the\n' + ':py:obj:`~.cudaLaunchAttributeValue.deviceUpdatableKernelNode.deviceUpdatable`\n' + 'can only be set to 0 or 1. Setting the field to 1 indicates that the\n' 'corresponding kernel node should be device-updatable. On success, a handle\n' 'will be returned via\n' ':py:obj:`~.cudaLaunchAttributeValue.deviceUpdatableKernelNode.devNode`\n' @@ -6835,8 +6835,8 @@ class cudaKernelNodeAttrID(_FastEnum): cyruntime.cudaLaunchAttributeID.cudaLaunchAttributeDeviceUpdatableKernelNode, 'Valid for graph nodes, launches. This attribute is graphs-only, and passing\n' 'it to a launch in a non-capturing stream will result in an error.\n' - ' :cudaLaunchAttributeValue::deviceUpdatableKernelNode::deviceUpdatable can\n' - 'only be set to 0 or 1. Setting the field to 1 indicates that the\n' + ':py:obj:`~.cudaLaunchAttributeValue.deviceUpdatableKernelNode.deviceUpdatable`\n' + 'can only be set to 0 or 1. Setting the field to 1 indicates that the\n' 'corresponding kernel node should be device-updatable. On success, a handle\n' 'will be returned via\n' ':py:obj:`~.cudaLaunchAttributeValue.deviceUpdatableKernelNode.devNode`\n' @@ -7919,10 +7919,6 @@ cdef class cudaArraySparseProperties: Flags will either be zero or cudaArraySparsePropertiesSingleMipTail - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -7969,12 +7965,6 @@ cdef class cudaArraySparseProperties: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -8011,14 +8001,6 @@ cdef class cudaArraySparseProperties: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class cudaArrayMemoryRequirements: """ CUDA array and CUDA mipmapped array memory requirements @@ -8034,10 +8016,6 @@ cdef class cudaArrayMemoryRequirements: Alignment necessary for mapping the array. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -8069,12 +8047,6 @@ cdef class cudaArrayMemoryRequirements: except ValueError: str_list += ['alignment : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -8095,14 +8067,6 @@ cdef class cudaArrayMemoryRequirements: self._pvt_ptr[0].alignment = alignment - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class cudaPitchedPtr: """ CUDA Pitched memory pointer make_cudaPitchedPtr @@ -8599,10 +8563,6 @@ cdef class cudaMemcpyNodeParams: Must be zero - reserved : int - Must be zero - - ctx : cudaExecutionContext_t Context in which to run the memcpy. If NULL will try to use the current context. @@ -8644,12 +8604,6 @@ cdef class cudaMemcpyNodeParams: str_list += ['flags : '] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - - try: str_list += ['ctx : ' + str(self.ctx)] except ValueError: @@ -8673,14 +8627,6 @@ cdef class cudaMemcpyNodeParams: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, int reserved): - self._pvt_ptr[0].reserved = reserved - - @property def ctx(self): return self._ctx @@ -9872,13 +9818,6 @@ cdef class anon_struct4: cdef class anon_struct5: """ - Attributes - ---------- - - reserved : list[int] - - - Methods ------- getPtr() @@ -9897,23 +9836,10 @@ cdef class anon_struct5: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return self._pvt_ptr[0].res.reserved.reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].res.reserved.reserved = reserved - - cdef class anon_union0: """ Attributes @@ -9935,10 +9861,6 @@ cdef class anon_union0: - reserved : anon_struct5 - - - Methods ------- getPtr() @@ -9961,9 +9883,6 @@ cdef class anon_union0: self._pitch2D = anon_struct4(_ptr=self._pvt_ptr) - - self._reserved = anon_struct5(_ptr=self._pvt_ptr) - def __dealloc__(self): pass def getPtr(self): @@ -9995,12 +9914,6 @@ cdef class anon_union0: except ValueError: str_list += ['pitch2D : '] - - try: - str_list += ['reserved :\n' + '\n'.join([' ' + line for line in str(self.reserved).splitlines()])] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -10037,14 +9950,6 @@ cdef class anon_union0: string.memcpy(&self._pvt_ptr[0].res.pitch2D, pitch2D.getPtr(), sizeof(self._pvt_ptr[0].res.pitch2D)) - @property - def reserved(self): - return self._reserved - @reserved.setter - def reserved(self, reserved not None : anon_struct5): - string.memcpy(&self._pvt_ptr[0].res.reserved, reserved.getPtr(), sizeof(self._pvt_ptr[0].res.reserved)) - - cdef class cudaResourceDesc: """ CUDA resource descriptor @@ -10173,10 +10078,6 @@ cdef class cudaResourceViewDesc: Last layer index - reserved : list[unsigned int] - Must be zero - - Methods ------- getPtr() @@ -10244,12 +10145,6 @@ cdef class cudaResourceViewDesc: except ValueError: str_list += ['lastLayer : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -10318,14 +10213,6 @@ cdef class cudaResourceViewDesc: self._pvt_ptr[0].lastLayer = lastLayer - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class cudaPointerAttributes: """ CUDA pointer attributes @@ -10360,10 +10247,6 @@ cdef class cudaPointerAttributes: pointer if an invalid pointer has been passed to CUDA. - reserved : list[long] - Must be zero - - Methods ------- getPtr() @@ -10407,12 +10290,6 @@ cdef class cudaPointerAttributes: except ValueError: str_list += ['hostPointer : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -10451,14 +10328,6 @@ cdef class cudaPointerAttributes: self._pvt_ptr[0].hostPointer = self._cyhostPointer.cptr - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class cudaFuncAttributes: """ CUDA function attributes @@ -10573,14 +10442,6 @@ cdef class cudaFuncAttributes: the value. - reserved1 : int - - - - reserved : list[int] - Reserved for future use. - - Methods ------- getPtr() @@ -10702,18 +10563,6 @@ cdef class cudaFuncAttributes: except ValueError: str_list += ['deviceNodeUpdateStatus : '] - - try: - str_list += ['reserved1 : ' + str(self.reserved1)] - except ValueError: - str_list += ['reserved1 : '] - - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -10854,22 +10703,6 @@ cdef class cudaFuncAttributes: self._pvt_ptr[0].deviceNodeUpdateStatus = deviceNodeUpdateStatus - @property - def reserved1(self): - return self._pvt_ptr[0].reserved1 - @reserved1.setter - def reserved1(self, int reserved1): - self._pvt_ptr[0].reserved1 = reserved1 - - - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class cudaMemLocation: """ Specifies a memory location. To specify a gpu, set type = @@ -11049,10 +10882,6 @@ cdef class cudaMemPoolProps: Bitmask indicating intended usage for the pool. - reserved : bytes - reserved for future use, must be 0 - - Methods ------- getPtr() @@ -11111,12 +10940,6 @@ cdef class cudaMemPoolProps: except ValueError: str_list += ['usage : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -11170,28 +10993,10 @@ cdef class cudaMemPoolProps: self._pvt_ptr[0].usage = usage - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 54) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 54: - raise ValueError("reserved length must be 54, is " + str(len(reserved))) - for i, b in enumerate(reserved): - self._pvt_ptr[0].reserved[i] = b - - cdef class cudaMemPoolPtrExportData: """ Opaque data for exporting a pool allocation - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -11212,26 +11017,10 @@ cdef class cudaMemPoolPtrExportData: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 64) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 64: - raise ValueError("reserved length must be 64, is " + str(len(reserved))) - for i, b in enumerate(reserved): - self._pvt_ptr[0].reserved[i] = b - - cdef class cudaMemAllocNodeParams: """ Memory allocation node parameters @@ -12663,10 +12452,6 @@ cdef class cudaDeviceProp: multi-node system. - reserved : list[int] - Reserved for future use - - Methods ------- getPtr() @@ -13241,12 +13026,6 @@ cdef class cudaDeviceProp: except ValueError: str_list += ['hostNumaMultinodeIpcSupported : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -13999,25 +13778,10 @@ cdef class cudaDeviceProp: self._pvt_ptr[0].hostNumaMultinodeIpcSupported = hostNumaMultinodeIpcSupported - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class cudaIpcEventHandle_st: """ CUDA IPC event handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -14038,45 +13802,14 @@ cdef class cudaIpcEventHandle_st: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 64) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 64: - raise ValueError("reserved length must be 64, is " + str(len(reserved))) - if CHAR_MIN == 0: - for i, b in enumerate(reserved): - if b < 0 and b > -129: - b = b + 256 - self._pvt_ptr[0].reserved[i] = b - else: - for i, b in enumerate(reserved): - if b > 127 and b < 256: - b = b - 256 - self._pvt_ptr[0].reserved[i] = b - - cdef class cudaIpcMemHandle_st: """ CUDA IPC memory handle - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -14097,43 +13830,12 @@ cdef class cudaIpcMemHandle_st: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 64) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 64: - raise ValueError("reserved length must be 64, is " + str(len(reserved))) - if CHAR_MIN == 0: - for i, b in enumerate(reserved): - if b < 0 and b > -129: - b = b + 256 - self._pvt_ptr[0].reserved[i] = b - else: - for i, b in enumerate(reserved): - if b > 127 and b < 256: - b = b - 256 - self._pvt_ptr[0].reserved[i] = b - - cdef class cudaMemFabricHandle_st: """ - Attributes - ---------- - - reserved : bytes - - - Methods ------- getPtr() @@ -14154,34 +13856,10 @@ cdef class cudaMemFabricHandle_st: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 64) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 64: - raise ValueError("reserved length must be 64, is " + str(len(reserved))) - if CHAR_MIN == 0: - for i, b in enumerate(reserved): - if b < 0 and b > -129: - b = b + 256 - self._pvt_ptr[0].reserved[i] = b - else: - for i, b in enumerate(reserved): - if b > 127 and b < 256: - b = b - 256 - self._pvt_ptr[0].reserved[i] = b - - cdef class anon_struct8: """ Attributes @@ -14353,10 +14031,6 @@ cdef class cudaExternalMemoryHandleDesc: Flags must either be zero or cudaExternalMemoryDedicated - reserved : list[unsigned int] - Must be zero - - Methods ------- getPtr() @@ -14405,12 +14079,6 @@ cdef class cudaExternalMemoryHandleDesc: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -14447,14 +14115,6 @@ cdef class cudaExternalMemoryHandleDesc: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class cudaExternalMemoryBufferDesc: """ External memory buffer descriptor @@ -14474,10 +14134,6 @@ cdef class cudaExternalMemoryBufferDesc: Flags reserved for future use. Must be zero. - reserved : list[unsigned int] - Must be zero - - Methods ------- getPtr() @@ -14515,12 +14171,6 @@ cdef class cudaExternalMemoryBufferDesc: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -14549,14 +14199,6 @@ cdef class cudaExternalMemoryBufferDesc: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class cudaExternalMemoryMipmappedArrayDesc: """ External memory mipmap descriptor @@ -14586,10 +14228,6 @@ cdef class cudaExternalMemoryMipmappedArrayDesc: Total number of levels in the mipmap chain - reserved : list[unsigned int] - Must be zero - - Methods ------- getPtr() @@ -14645,12 +14283,6 @@ cdef class cudaExternalMemoryMipmappedArrayDesc: except ValueError: str_list += ['numLevels : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -14695,14 +14327,6 @@ cdef class cudaExternalMemoryMipmappedArrayDesc: self._pvt_ptr[0].numLevels = numLevels - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class anon_struct9: """ Attributes @@ -14870,10 +14494,6 @@ cdef class cudaExternalSemaphoreHandleDesc: Flags reserved for the future. Must be zero. - reserved : list[unsigned int] - Must be zero - - Methods ------- getPtr() @@ -14916,12 +14536,6 @@ cdef class cudaExternalSemaphoreHandleDesc: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -14950,14 +14564,6 @@ cdef class cudaExternalSemaphoreHandleDesc: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class anon_struct10: """ Attributes @@ -15011,10 +14617,6 @@ cdef class anon_union5: - reserved : unsigned long long - - - Methods ------- getPtr() @@ -15038,12 +14640,6 @@ cdef class anon_union5: except ValueError: str_list += ['fence : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -15057,14 +14653,6 @@ cdef class anon_union5: self._pvt_ptr[0].params.nvSciSync.fence = self._cyfence.cptr - @property - def reserved(self): - return self._pvt_ptr[0].params.nvSciSync.reserved - @reserved.setter - def reserved(self, unsigned long long reserved): - self._pvt_ptr[0].params.nvSciSync.reserved = reserved - - cdef class anon_struct11: """ Attributes @@ -15126,10 +14714,6 @@ cdef class anon_struct12: - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -15174,12 +14758,6 @@ cdef class anon_struct12: except ValueError: str_list += ['keyedMutex : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -15208,14 +14786,6 @@ cdef class anon_struct12: string.memcpy(&self._pvt_ptr[0].params.keyedMutex, keyedMutex.getPtr(), sizeof(self._pvt_ptr[0].params.keyedMutex)) - @property - def reserved(self): - return self._pvt_ptr[0].params.reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].params.reserved = reserved - - cdef class cudaExternalSemaphoreSignalParams: """ External semaphore signal parameters, compatible with driver type @@ -15238,10 +14808,6 @@ cdef class cudaExternalSemaphoreSignalParams: all other types of cudaExternalSemaphore_t, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -15276,12 +14842,6 @@ cdef class cudaExternalSemaphoreSignalParams: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -15302,14 +14862,6 @@ cdef class cudaExternalSemaphoreSignalParams: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class anon_struct13: """ Attributes @@ -15363,10 +14915,6 @@ cdef class anon_union6: - reserved : unsigned long long - - - Methods ------- getPtr() @@ -15390,12 +14938,6 @@ cdef class anon_union6: except ValueError: str_list += ['fence : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -15409,14 +14951,6 @@ cdef class anon_union6: self._pvt_ptr[0].params.nvSciSync.fence = self._cyfence.cptr - @property - def reserved(self): - return self._pvt_ptr[0].params.nvSciSync.reserved - @reserved.setter - def reserved(self, unsigned long long reserved): - self._pvt_ptr[0].params.nvSciSync.reserved = reserved - - cdef class anon_struct14: """ Attributes @@ -15496,10 +15030,6 @@ cdef class anon_struct15: - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -15544,12 +15074,6 @@ cdef class anon_struct15: except ValueError: str_list += ['keyedMutex : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -15578,14 +15102,6 @@ cdef class anon_struct15: string.memcpy(&self._pvt_ptr[0].params.keyedMutex, keyedMutex.getPtr(), sizeof(self._pvt_ptr[0].params.keyedMutex)) - @property - def reserved(self): - return self._pvt_ptr[0].params.reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].params.reserved = reserved - - cdef class cudaExternalSemaphoreWaitParams: """ External semaphore wait parameters, compatible with driver type @@ -15608,10 +15124,6 @@ cdef class cudaExternalSemaphoreWaitParams: all other types of cudaExternalSemaphore_t, flags must be zero. - reserved : list[unsigned int] - - - Methods ------- getPtr() @@ -15646,12 +15158,6 @@ cdef class cudaExternalSemaphoreWaitParams: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -15672,14 +15178,6 @@ cdef class cudaExternalSemaphoreWaitParams: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class cudaDevSmResource: """ Data for SM-related resources All parameters in this structure are @@ -15876,13 +15374,6 @@ cdef class cudaDevWorkqueueResource: """ Handle to a pre-existing workqueue related resource - Attributes - ---------- - - reserved : bytes - Reserved for future use - - Methods ------- getPtr() @@ -15903,26 +15394,10 @@ cdef class cudaDevWorkqueueResource: if self._pvt_ptr is not NULL: str_list = [] - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 40) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 40: - raise ValueError("reserved length must be 40, is " + str(len(reserved))) - for i, b in enumerate(reserved): - self._pvt_ptr[0].reserved[i] = b - - cdef class cudaDevSmResourceGroupParams_st: """ Input data for splitting SMs @@ -15949,10 +15424,6 @@ cdef class cudaDevSmResourceGroupParams_st: this this group is created. - reserved : list[unsigned int] - Reserved for future use - ensure this is zero initialized. - - Methods ------- getPtr() @@ -15996,12 +15467,6 @@ cdef class cudaDevSmResourceGroupParams_st: except ValueError: str_list += ['flags : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -16038,14 +15503,6 @@ cdef class cudaDevSmResourceGroupParams_st: self._pvt_ptr[0].flags = flags - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class cudaDevResource_st: """ A tagged union describing different resources identified by the @@ -17642,14 +17099,6 @@ cdef class cudaGraphNodeParams: Type of the node - reserved0 : list[int] - Reserved. Must be zero. - - - reserved1 : list[long long] - Padding. Unused bytes must be zero. - - kernel : cudaKernelNodeParamsV2 Kernel node parameters. @@ -17698,10 +17147,6 @@ cdef class cudaGraphNodeParams: Conditional node parameters. - reserved2 : long long - Reserved bytes. Must be zero. - - Methods ------- getPtr() @@ -17766,18 +17211,6 @@ cdef class cudaGraphNodeParams: str_list += ['type : '] - try: - str_list += ['reserved0 : ' + str(self.reserved0)] - except ValueError: - str_list += ['reserved0 : '] - - - try: - str_list += ['reserved1 : ' + str(self.reserved1)] - except ValueError: - str_list += ['reserved1 : '] - - try: str_list += ['kernel :\n' + '\n'.join([' ' + line for line in str(self.kernel).splitlines()])] except ValueError: @@ -17849,12 +17282,6 @@ cdef class cudaGraphNodeParams: except ValueError: str_list += ['conditional : '] - - try: - str_list += ['reserved2 : ' + str(self.reserved2)] - except ValueError: - str_list += ['reserved2 : '] - return '\n'.join(str_list) else: return '' @@ -17867,22 +17294,6 @@ cdef class cudaGraphNodeParams: self._pvt_ptr[0].type = int(type) - @property - def reserved0(self): - return self._pvt_ptr[0].reserved0 - @reserved0.setter - def reserved0(self, reserved0): - self._pvt_ptr[0].reserved0 = reserved0 - - - @property - def reserved1(self): - return self._pvt_ptr[0].reserved1 - @reserved1.setter - def reserved1(self, reserved1): - self._pvt_ptr[0].reserved1 = reserved1 - - @property def kernel(self): return self._kernel @@ -17979,14 +17390,6 @@ cdef class cudaGraphNodeParams: string.memcpy(&self._pvt_ptr[0].conditional, conditional.getPtr(), sizeof(self._pvt_ptr[0].conditional)) - @property - def reserved2(self): - return self._pvt_ptr[0].reserved2 - @reserved2.setter - def reserved2(self, long long reserved2): - self._pvt_ptr[0].reserved2 = reserved2 - - cdef class cudaGraphEdgeData_st: """ Optional annotation for edges in a CUDA graph. Note, all edges @@ -18024,11 +17427,6 @@ cdef class cudaGraphEdgeData_st: See cudaGraphDependencyType. - reserved : bytes - These bytes are unused and must be zeroed. This ensures - compatibility if additional fields are added in the future. - - Methods ------- getPtr() @@ -18066,12 +17464,6 @@ cdef class cudaGraphEdgeData_st: except ValueError: str_list += ['type : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -18100,17 +17492,6 @@ cdef class cudaGraphEdgeData_st: self._pvt_ptr[0].type = type - @property - def reserved(self): - return PyBytes_FromStringAndSize(self._pvt_ptr[0].reserved, 5) - @reserved.setter - def reserved(self, reserved): - if len(reserved) != 5: - raise ValueError("reserved length must be 5, is " + str(len(reserved))) - for i, b in enumerate(reserved): - self._pvt_ptr[0].reserved[i] = b - - cdef class cudaGraphInstantiateParams_st: """ Graph instantiation parameters @@ -19167,12 +18548,12 @@ cdef class cudaLaunchAttributeValue: with the following fields: - `x` - The X dimension of the preferred cluster, in blocks. Must be a divisor of the grid X dimension, and must be a multiple of the `x` field of - ::cudaLaunchAttributeValue::clusterDim. - `y` - The Y dimension - of the preferred cluster, in blocks. Must be a divisor of the grid - Y dimension, and must be a multiple of the `y` field of - ::cudaLaunchAttributeValue::clusterDim. - `z` - The Z dimension - of the preferred cluster, in blocks. Must be equal to the `z` field - of ::cudaLaunchAttributeValue::clusterDim. + cudaLaunchAttributeValue::clusterDim. - `y` - The Y dimension of + the preferred cluster, in blocks. Must be a divisor of the grid Y + dimension, and must be a multiple of the `y` field of + cudaLaunchAttributeValue::clusterDim. - `z` - The Z dimension of + the preferred cluster, in blocks. Must be equal to the `z` field of + cudaLaunchAttributeValue::clusterDim. launchCompletionEvent : anon_struct20 @@ -20127,10 +19508,6 @@ cdef class cudaEglPlaneDesc_st: Channel Format Descriptor - reserved : list[unsigned int] - Reserved for future use - - Methods ------- getPtr() @@ -20189,12 +19566,6 @@ cdef class cudaEglPlaneDesc_st: except ValueError: str_list += ['channelDesc : '] - - try: - str_list += ['reserved : ' + str(self.reserved)] - except ValueError: - str_list += ['reserved : '] - return '\n'.join(str_list) else: return '' @@ -20247,14 +19618,6 @@ cdef class cudaEglPlaneDesc_st: string.memcpy(&self._pvt_ptr[0].channelDesc, channelDesc.getPtr(), sizeof(self._pvt_ptr[0].channelDesc)) - @property - def reserved(self): - return self._pvt_ptr[0].reserved - @reserved.setter - def reserved(self, reserved): - self._pvt_ptr[0].reserved = reserved - - cdef class anon_union12: """ Attributes diff --git a/cuda_bindings/docs/source/module/runtime.rst b/cuda_bindings/docs/source/module/runtime.rst index 80b11f16644..000c5fa188f 100644 --- a/cuda_bindings/docs/source/module/runtime.rst +++ b/cuda_bindings/docs/source/module/runtime.rst @@ -1,7 +1,7 @@ .. SPDX-FileCopyrightText: Copyright (c) 2021-2026 NVIDIA CORPORATION & AFFILIATES. All rights reserved. .. SPDX-License-Identifier: Apache-2.0 -.. CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=0eccd5db44f7406acb693f5dd95ad2fa17c787c11659578cf54e116eb0b06e01 +.. CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=86b1e47dc2cb6ed343cc979b646bdfb99db65d352605464573a8e1d5b248fce2 ------- runtime ------- @@ -4185,7 +4185,7 @@ Data types used by CUDA Runtime Valid for graph nodes, launches. This attribute is graphs-only, and passing it to a launch in a non-capturing stream will result in an error. - :cudaLaunchAttributeValue::deviceUpdatableKernelNode::deviceUpdatable can only be set to 0 or 1. Setting the field to 1 indicates that the corresponding kernel node should be device-updatable. On success, a handle will be returned via :py:obj:`~.cudaLaunchAttributeValue.deviceUpdatableKernelNode.devNode` which can be passed to the various device-side update functions to update the node's kernel parameters from within another kernel. For more information on the types of device updates that can be made, as well as the relevant limitations thereof, see :py:obj:`~.cudaGraphKernelNodeUpdatesApply`. + :py:obj:`~.cudaLaunchAttributeValue.deviceUpdatableKernelNode.deviceUpdatable` can only be set to 0 or 1. Setting the field to 1 indicates that the corresponding kernel node should be device-updatable. On success, a handle will be returned via :py:obj:`~.cudaLaunchAttributeValue.deviceUpdatableKernelNode.devNode` which can be passed to the various device-side update functions to update the node's kernel parameters from within another kernel. For more information on the types of device updates that can be made, as well as the relevant limitations thereof, see :py:obj:`~.cudaGraphKernelNodeUpdatesApply`. Nodes which are device-updatable have additional restrictions compared to regular kernel nodes. Firstly, device-updatable nodes cannot be removed from their graph via :py:obj:`~.cudaGraphDestroyNode`. Additionally, once opted-in to this functionality, a node cannot opt out, and any attempt to set the deviceUpdatable attribute to 0 will result in an error. Device-updatable kernel nodes also cannot have their attributes copied to/from another kernel node via :py:obj:`~.cudaGraphKernelNodeCopyAttributes`. Graphs containing one or more device-updatable nodes also do not allow multiple instantiation, and neither the graph nor its instantiated version can be passed to :py:obj:`~.cudaGraphExecUpdate`.