From c0248faa863190718c4ec1b18d178d5eead6f38f Mon Sep 17 00:00:00 2001 From: "Ralf W. Grosse-Kunstleve" Date: Fri, 25 Sep 2026 21:57:43 -0700 Subject: [PATCH 1/5] run_cybind_cython_gen 13.4.2 ../post_mr574_public_refresh (NO MANUAL CHANGES) --- cuda_bindings/cuda/bindings/cyruntime.pxd | 5 +- cuda_bindings/cuda/bindings/driver.pxd | 143 +++- cuda_bindings/cuda/bindings/driver.pyx | 834 +++++++--------------- cuda_bindings/cuda/bindings/nvrtc.pxd | 3 +- cuda_bindings/cuda/bindings/runtime.pxd | 105 ++- cuda_bindings/cuda/bindings/runtime.pyx | 601 ++++++---------- 6 files changed, 721 insertions(+), 970 deletions(-) diff --git a/cuda_bindings/cuda/bindings/cyruntime.pxd b/cuda_bindings/cuda/bindings/cyruntime.pxd index 2d705a6be16..3bd31653dd3 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.4.1. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=c3643e519b69bdb09b9c4c6ff3ecd3aebb180636d00e9a7bd2fe129cbed3eeb4 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=f18e04577ef4372076f7baaf4adeeb91967e3c809bfdd0e4b1224d0d9ded81e2 from libc.stdint cimport uint32_t, uint64_t @@ -2674,6 +2674,9 @@ cdef extern from 'cuda_runtime_api.h': cdef enum: CUDA_EGL_MAX_PLANES = 3 +# cudaDevSmResourceGroupLocalityDomainIdAny is defined as (~0u) in driver_types.h; the +# pyclibrary-based cython-gen parser can't evaluate that expression, so hardcode the value + # libraryPropertyType_t (starts lowercase, outside type pattern) cdef extern from 'library_types.h': ctypedef enum libraryPropertyType_t 'libraryPropertyType_t': diff --git a/cuda_bindings/cuda/bindings/driver.pxd b/cuda_bindings/cuda/bindings/driver.pxd index 454c4cd7e59..6f328056ca1 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.4.1. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=4f3e3117475b43ef1ebbe0cd972d2aa6ef4dc5d449a43f1d9ad1d01625604c32 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=335719e84ce1d6e1fcd12d7a0d627d5c7f8be1a80379cae902ebe72fa3b1a03f cimport cuda.bindings.cydriver as cydriver include "_lib/utils.pxd" @@ -530,6 +530,7 @@ cdef class CUuuid_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUuuid_st _pvt_val cdef cydriver.CUuuid_st* _pvt_ptr @@ -552,6 +553,7 @@ cdef class CUmemFabricHandle_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemFabricHandle_st _pvt_val cdef cydriver.CUmemFabricHandle_st* _pvt_ptr @@ -564,6 +566,7 @@ cdef class CUipcEventHandle_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUipcEventHandle_st _pvt_val cdef cydriver.CUipcEventHandle_st* _pvt_ptr @@ -576,6 +579,7 @@ cdef class CUipcMemHandle_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUipcMemHandle_st _pvt_val cdef cydriver.CUipcMemHandle_st* _pvt_ptr @@ -613,6 +617,7 @@ cdef class CUstreamMemOpWaitValueParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUstreamBatchMemOpParams_union* _pvt_ptr cdef CUdeviceptr _address @@ -661,6 +666,7 @@ cdef class CUstreamMemOpWriteValueParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUstreamBatchMemOpParams_union* _pvt_ptr cdef CUdeviceptr _address @@ -693,6 +699,7 @@ cdef class CUstreamMemOpFlushRemoteWritesParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUstreamBatchMemOpParams_union* _pvt_ptr cdef class CUstreamMemOpMemoryBarrierParams_st: @@ -713,6 +720,7 @@ cdef class CUstreamMemOpMemoryBarrierParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUstreamBatchMemOpParams_union* _pvt_ptr cdef class CUstreamMemOpAtomicReductionParams_st: @@ -753,6 +761,7 @@ cdef class CUstreamMemOpAtomicReductionParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUstreamBatchMemOpParams_union* _pvt_ptr cdef CUdeviceptr _address @@ -807,6 +816,7 @@ cdef class CUstreamBatchMemOpParams_union: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUstreamBatchMemOpParams_union _pvt_val cdef cydriver.CUstreamBatchMemOpParams_union* _pvt_ptr @@ -854,6 +864,7 @@ cdef class CUDA_BATCH_MEM_OP_NODE_PARAMS_v1_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_BATCH_MEM_OP_NODE_PARAMS_v1_st _pvt_val cdef cydriver.CUDA_BATCH_MEM_OP_NODE_PARAMS_v1_st* _pvt_ptr @@ -892,6 +903,7 @@ cdef class CUDA_BATCH_MEM_OP_NODE_PARAMS_v2_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_BATCH_MEM_OP_NODE_PARAMS_v2_st _pvt_val cdef cydriver.CUDA_BATCH_MEM_OP_NODE_PARAMS_v2_st* _pvt_ptr @@ -916,6 +928,7 @@ cdef class anon_struct0: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUasyncNotificationInfo_st* _pvt_ptr cdef class anon_union2: @@ -932,6 +945,7 @@ cdef class anon_union2: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUasyncNotificationInfo_st* _pvt_ptr cdef anon_struct0 _overBudget @@ -958,6 +972,7 @@ cdef class CUasyncNotificationInfo_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUasyncNotificationInfo_st* _val_ptr cdef cydriver.CUasyncNotificationInfo_st* _pvt_ptr @@ -1016,6 +1031,7 @@ cdef class CUdevprop_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUdevprop_st _pvt_val cdef cydriver.CUdevprop_st* _pvt_ptr @@ -1063,6 +1079,7 @@ cdef class CUaccessPolicyWindow_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUaccessPolicyWindow_st _pvt_val cdef cydriver.CUaccessPolicyWindow_st* _pvt_ptr @@ -1121,6 +1138,7 @@ cdef class CUDA_KERNEL_NODE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_KERNEL_NODE_PARAMS_st _pvt_val cdef cydriver.CUDA_KERNEL_NODE_PARAMS_st* _pvt_ptr @@ -1192,6 +1210,7 @@ cdef class CUDA_KERNEL_NODE_PARAMS_v2_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_KERNEL_NODE_PARAMS_v2_st _pvt_val cdef cydriver.CUDA_KERNEL_NODE_PARAMS_v2_st* _pvt_ptr @@ -1269,6 +1288,7 @@ cdef class CUDA_KERNEL_NODE_PARAMS_v3_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_KERNEL_NODE_PARAMS_v3_st _pvt_val cdef cydriver.CUDA_KERNEL_NODE_PARAMS_v3_st* _pvt_ptr @@ -1320,6 +1340,7 @@ cdef class CUDA_MEMSET_NODE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_MEMSET_NODE_PARAMS_st _pvt_val cdef cydriver.CUDA_MEMSET_NODE_PARAMS_st* _pvt_ptr @@ -1366,6 +1387,7 @@ cdef class CUDA_MEMSET_NODE_PARAMS_v2_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_MEMSET_NODE_PARAMS_v2_st _pvt_val cdef cydriver.CUDA_MEMSET_NODE_PARAMS_v2_st* _pvt_ptr @@ -1395,6 +1417,7 @@ cdef class CUDA_HOST_NODE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_HOST_NODE_PARAMS_st _pvt_val cdef cydriver.CUDA_HOST_NODE_PARAMS_st* _pvt_ptr @@ -1436,6 +1459,7 @@ cdef class CUDA_HOST_NODE_PARAMS_v2_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_HOST_NODE_PARAMS_v2_st* _val_ptr cdef cydriver.CUDA_HOST_NODE_PARAMS_v2_st* _pvt_ptr @@ -1502,6 +1526,7 @@ cdef class CUDA_CONDITIONAL_NODE_PARAMS: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_CONDITIONAL_NODE_PARAMS _pvt_val cdef cydriver.CUDA_CONDITIONAL_NODE_PARAMS* _pvt_ptr @@ -1557,6 +1582,7 @@ cdef class CUgraphEdgeData_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUgraphEdgeData_st _pvt_val cdef cydriver.CUgraphEdgeData_st* _pvt_ptr @@ -1588,6 +1614,7 @@ cdef class CUDA_GRAPH_INSTANTIATE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_GRAPH_INSTANTIATE_PARAMS_st _pvt_val cdef cydriver.CUDA_GRAPH_INSTANTIATE_PARAMS_st* _pvt_ptr @@ -1626,6 +1653,7 @@ cdef class CUlaunchMemSyncDomainMap_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlaunchMemSyncDomainMap_st _pvt_val cdef cydriver.CUlaunchMemSyncDomainMap_st* _pvt_ptr @@ -1651,6 +1679,7 @@ cdef class anon_struct1: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlaunchAttributeValue_union* _pvt_ptr cdef class anon_struct2: @@ -1675,6 +1704,7 @@ cdef class anon_struct2: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlaunchAttributeValue_union* _pvt_ptr cdef CUevent _event @@ -1698,6 +1728,7 @@ cdef class anon_struct3: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlaunchAttributeValue_union* _pvt_ptr cdef CUevent _event @@ -1725,6 +1756,7 @@ cdef class anon_struct4: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlaunchAttributeValue_union* _pvt_ptr cdef class anon_struct5: @@ -1745,6 +1777,7 @@ cdef class anon_struct5: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlaunchAttributeValue_union* _pvt_ptr cdef CUgraphDeviceNode _devNode @@ -1877,6 +1910,7 @@ cdef class CUlaunchAttributeValue_union: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlaunchAttributeValue_union _pvt_val cdef cydriver.CUlaunchAttributeValue_union* _pvt_ptr @@ -1921,6 +1955,7 @@ cdef class CUlaunchAttribute_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlaunchAttribute_st _pvt_val cdef cydriver.CUlaunchAttribute_st* _pvt_ptr @@ -1979,6 +2014,7 @@ cdef class CUlaunchConfig_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlaunchConfig_st _pvt_val cdef cydriver.CUlaunchConfig_st* _pvt_ptr @@ -2005,6 +2041,7 @@ cdef class CUexecAffinitySmCount_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUexecAffinitySmCount_st _pvt_val cdef cydriver.CUexecAffinitySmCount_st* _pvt_ptr @@ -2022,6 +2059,7 @@ cdef class anon_union4: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUexecAffinityParam_st* _pvt_ptr cdef CUexecAffinitySmCount _smCount @@ -2047,6 +2085,7 @@ cdef class CUexecAffinityParam_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUexecAffinityParam_st* _val_ptr cdef cydriver.CUexecAffinityParam_st* _pvt_ptr @@ -2074,6 +2113,7 @@ cdef class CUctxCigParam_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUctxCigParam_st _pvt_val cdef cydriver.CUctxCigParam_st* _pvt_ptr @@ -2111,6 +2151,7 @@ cdef class CUctxCreateParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUctxCreateParams_st _pvt_val cdef cydriver.CUctxCreateParams_st* _pvt_ptr @@ -2143,6 +2184,7 @@ cdef class CUstreamCigParam_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUstreamCigParam_st _pvt_val cdef cydriver.CUstreamCigParam_st* _pvt_ptr @@ -2167,6 +2209,7 @@ cdef class CUstreamCigCaptureParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUstreamCigCaptureParams_st _pvt_val cdef cydriver.CUstreamCigCaptureParams_st* _pvt_ptr @@ -2200,6 +2243,7 @@ cdef class CUlibraryHostUniversalFunctionAndDataTable_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlibraryHostUniversalFunctionAndDataTable_st _pvt_val cdef cydriver.CUlibraryHostUniversalFunctionAndDataTable_st* _pvt_ptr @@ -2285,6 +2329,7 @@ cdef class CUDA_MEMCPY2D_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_MEMCPY2D_st _pvt_val cdef cydriver.CUDA_MEMCPY2D_st* _pvt_ptr @@ -2411,6 +2456,7 @@ cdef class CUDA_MEMCPY3D_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_MEMCPY3D_st _pvt_val cdef cydriver.CUDA_MEMCPY3D_st* _pvt_ptr @@ -2546,6 +2592,7 @@ cdef class CUDA_MEMCPY3D_PEER_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_MEMCPY3D_PEER_st _pvt_val cdef cydriver.CUDA_MEMCPY3D_PEER_st* _pvt_ptr @@ -2597,6 +2644,7 @@ cdef class CUDA_MEMCPY_NODE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_MEMCPY_NODE_PARAMS_st _pvt_val cdef cydriver.CUDA_MEMCPY_NODE_PARAMS_st* _pvt_ptr @@ -2634,6 +2682,7 @@ cdef class CUDA_ARRAY_DESCRIPTOR_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_ARRAY_DESCRIPTOR_st _pvt_val cdef cydriver.CUDA_ARRAY_DESCRIPTOR_st* _pvt_ptr @@ -2673,6 +2722,7 @@ cdef class CUDA_ARRAY3D_DESCRIPTOR_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_ARRAY3D_DESCRIPTOR_st _pvt_val cdef cydriver.CUDA_ARRAY3D_DESCRIPTOR_st* _pvt_ptr @@ -2698,6 +2748,7 @@ cdef class anon_struct6: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_ARRAY_SPARSE_PROPERTIES_st* _pvt_ptr cdef class CUDA_ARRAY_SPARSE_PROPERTIES_st: @@ -2729,6 +2780,7 @@ cdef class CUDA_ARRAY_SPARSE_PROPERTIES_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_ARRAY_SPARSE_PROPERTIES_st _pvt_val cdef cydriver.CUDA_ARRAY_SPARSE_PROPERTIES_st* _pvt_ptr @@ -2755,6 +2807,7 @@ cdef class CUDA_ARRAY_MEMORY_REQUIREMENTS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_ARRAY_MEMORY_REQUIREMENTS_st _pvt_val cdef cydriver.CUDA_ARRAY_MEMORY_REQUIREMENTS_st* _pvt_ptr @@ -2772,6 +2825,7 @@ cdef class anon_struct7: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_RESOURCE_DESC_st* _pvt_ptr cdef CUarray _hArray @@ -2791,6 +2845,7 @@ cdef class anon_struct8: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_RESOURCE_DESC_st* _pvt_ptr cdef CUmipmappedArray _hMipmappedArray @@ -2822,6 +2877,7 @@ cdef class anon_struct9: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_RESOURCE_DESC_st* _pvt_ptr cdef CUdeviceptr _devPtr @@ -2861,6 +2917,7 @@ cdef class anon_struct10: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_RESOURCE_DESC_st* _pvt_ptr cdef CUdeviceptr _devPtr @@ -2873,6 +2930,7 @@ cdef class anon_struct11: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_RESOURCE_DESC_st* _pvt_ptr cdef class anon_union5: @@ -2901,6 +2959,7 @@ cdef class anon_union5: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_RESOURCE_DESC_st* _pvt_ptr cdef anon_struct7 _array @@ -2939,6 +2998,7 @@ cdef class CUDA_RESOURCE_DESC_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_RESOURCE_DESC_st* _val_ptr cdef cydriver.CUDA_RESOURCE_DESC_st* _pvt_ptr @@ -2993,6 +3053,7 @@ cdef class CUDA_TEXTURE_DESC_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_TEXTURE_DESC_st _pvt_val cdef cydriver.CUDA_TEXTURE_DESC_st* _pvt_ptr @@ -3040,6 +3101,7 @@ cdef class CUDA_RESOURCE_VIEW_DESC_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_RESOURCE_VIEW_DESC_st _pvt_val cdef cydriver.CUDA_RESOURCE_VIEW_DESC_st* _pvt_ptr @@ -3060,6 +3122,7 @@ cdef class CUtensorMap_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUtensorMap_st _pvt_val cdef cydriver.CUtensorMap_st* _pvt_ptr @@ -3083,6 +3146,7 @@ cdef class CUDA_POINTER_ATTRIBUTE_P2P_TOKENS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_POINTER_ATTRIBUTE_P2P_TOKENS_st _pvt_val cdef cydriver.CUDA_POINTER_ATTRIBUTE_P2P_TOKENS_st* _pvt_ptr @@ -3138,6 +3202,7 @@ cdef class CUDA_LAUNCH_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_LAUNCH_PARAMS_st _pvt_val cdef cydriver.CUDA_LAUNCH_PARAMS_st* _pvt_ptr @@ -3168,6 +3233,7 @@ cdef class anon_struct12: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st* _pvt_ptr cdef _HelperInputVoidPtr _cyhandle @@ -3198,6 +3264,7 @@ cdef class anon_union6: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st* _pvt_ptr cdef anon_struct12 _win32 @@ -3234,6 +3301,7 @@ cdef class CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st* _val_ptr cdef cydriver.CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st* _pvt_ptr @@ -3264,6 +3332,7 @@ cdef class CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st _pvt_val cdef cydriver.CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st* _pvt_ptr @@ -3292,6 +3361,7 @@ cdef class CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st _pvt_val cdef cydriver.CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st* _pvt_ptr @@ -3316,6 +3386,7 @@ cdef class anon_struct13: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st* _pvt_ptr cdef _HelperInputVoidPtr _cyhandle @@ -3346,6 +3417,7 @@ cdef class anon_union7: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st* _pvt_ptr cdef anon_struct13 _win32 @@ -3378,6 +3450,7 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st* _val_ptr cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st* _pvt_ptr @@ -3398,6 +3471,7 @@ cdef class anon_struct14: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st* _pvt_ptr cdef class anon_union8: @@ -3414,6 +3488,7 @@ cdef class anon_union8: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st* _pvt_ptr cdef _HelperInputVoidPtr _cyfence @@ -3433,6 +3508,7 @@ cdef class anon_struct15: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st* _pvt_ptr cdef class anon_struct16: @@ -3457,6 +3533,7 @@ cdef class anon_struct16: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st* _pvt_ptr cdef anon_struct14 _fence @@ -3495,6 +3572,7 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st _pvt_val cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st* _pvt_ptr @@ -3515,6 +3593,7 @@ cdef class anon_struct17: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st* _pvt_ptr cdef class anon_union9: @@ -3531,6 +3610,7 @@ cdef class anon_union9: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st* _pvt_ptr cdef _HelperInputVoidPtr _cyfence @@ -3554,6 +3634,7 @@ cdef class anon_struct18: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st* _pvt_ptr cdef class anon_struct19: @@ -3578,6 +3659,7 @@ cdef class anon_struct19: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st* _pvt_ptr cdef anon_struct17 _fence @@ -3616,6 +3698,7 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st _pvt_val cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st* _pvt_ptr @@ -3647,6 +3730,7 @@ cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st _pvt_val cdef cydriver.CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st* _pvt_ptr @@ -3691,6 +3775,7 @@ cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2_st* _val_ptr cdef cydriver.CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2_st* _pvt_ptr @@ -3733,6 +3818,7 @@ cdef class CUDA_EXT_SEM_WAIT_NODE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXT_SEM_WAIT_NODE_PARAMS_st _pvt_val cdef cydriver.CUDA_EXT_SEM_WAIT_NODE_PARAMS_st* _pvt_ptr @@ -3777,6 +3863,7 @@ cdef class CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2_st* _val_ptr cdef cydriver.CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2_st* _pvt_ptr @@ -3812,6 +3899,7 @@ cdef class anon_union12: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUarrayMapInfo_st* _pvt_ptr cdef CUmipmappedArray _mipmap @@ -3862,6 +3950,7 @@ cdef class anon_struct20: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUarrayMapInfo_st* _pvt_ptr cdef class anon_struct21: @@ -3886,6 +3975,7 @@ cdef class anon_struct21: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUarrayMapInfo_st* _pvt_ptr cdef class anon_union13: @@ -3906,6 +3996,7 @@ cdef class anon_union13: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUarrayMapInfo_st* _pvt_ptr cdef anon_struct20 _sparseLevel @@ -3928,6 +4019,7 @@ cdef class anon_union14: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUarrayMapInfo_st* _pvt_ptr cdef CUmemGenericAllocationHandle _memHandle @@ -3986,6 +4078,7 @@ cdef class CUarrayMapInfo_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUarrayMapInfo_st* _val_ptr cdef cydriver.CUarrayMapInfo_st* _pvt_ptr @@ -4016,6 +4109,7 @@ cdef class anon_struct22: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemLocation_st* _pvt_ptr cdef class CUmemLocation_st: @@ -4045,6 +4139,7 @@ cdef class CUmemLocation_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemLocation_st* _val_ptr cdef cydriver.CUmemLocation_st* _pvt_ptr @@ -4073,6 +4168,7 @@ cdef class anon_struct23: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemAllocationProp_st* _pvt_ptr cdef class CUmemAllocationProp_st: @@ -4111,6 +4207,7 @@ cdef class CUmemAllocationProp_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemAllocationProp_st _pvt_val cdef cydriver.CUmemAllocationProp_st* _pvt_ptr @@ -4154,6 +4251,7 @@ cdef class CUmulticastObjectProp_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmulticastObjectProp_st _pvt_val cdef cydriver.CUmulticastObjectProp_st* _pvt_ptr @@ -4177,6 +4275,7 @@ cdef class CUmemAccessDesc_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemAccessDesc_st _pvt_val cdef cydriver.CUmemAccessDesc_st* _pvt_ptr @@ -4210,6 +4309,7 @@ cdef class CUgraphExecUpdateResultInfo_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUgraphExecUpdateResultInfo_st _pvt_val cdef cydriver.CUgraphExecUpdateResultInfo_st* _pvt_ptr @@ -4279,6 +4379,7 @@ cdef class CUmemPoolProps_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemPoolProps_st _pvt_val cdef cydriver.CUmemPoolProps_st* _pvt_ptr @@ -4297,6 +4398,7 @@ cdef class CUmemPoolPtrExportData_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemPoolPtrExportData_st _pvt_val cdef cydriver.CUmemPoolPtrExportData_st* _pvt_ptr @@ -4332,6 +4434,7 @@ cdef class CUmemcpyAttributes_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemcpyAttributes_st _pvt_val cdef cydriver.CUmemcpyAttributes_st* _pvt_ptr @@ -4365,6 +4468,7 @@ cdef class CUoffset3D_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUoffset3D_st _pvt_val cdef cydriver.CUoffset3D_st* _pvt_ptr @@ -4392,6 +4496,7 @@ cdef class CUextent3D_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUextent3D_st _pvt_val cdef cydriver.CUextent3D_st* _pvt_ptr @@ -4421,6 +4526,7 @@ cdef class anon_struct24: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemcpy3DOperand_st* _pvt_ptr cdef CUdeviceptr _ptr @@ -4447,6 +4553,7 @@ cdef class anon_struct25: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemcpy3DOperand_st* _pvt_ptr cdef CUarray _array @@ -4473,6 +4580,7 @@ cdef class anon_union16: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemcpy3DOperand_st* _pvt_ptr cdef anon_struct24 _ptr @@ -4501,6 +4609,7 @@ cdef class CUmemcpy3DOperand_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemcpy3DOperand_st* _val_ptr cdef cydriver.CUmemcpy3DOperand_st* _pvt_ptr @@ -4538,6 +4647,7 @@ cdef class CUDA_MEMCPY3D_BATCH_OP_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_MEMCPY3D_BATCH_OP_st _pvt_val cdef cydriver.CUDA_MEMCPY3D_BATCH_OP_st* _pvt_ptr @@ -4586,6 +4696,7 @@ cdef class CUDA_MEM_ALLOC_NODE_PARAMS_v1_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_MEM_ALLOC_NODE_PARAMS_v1_st _pvt_val cdef cydriver.CUDA_MEM_ALLOC_NODE_PARAMS_v1_st* _pvt_ptr @@ -4635,6 +4746,7 @@ cdef class CUDA_MEM_ALLOC_NODE_PARAMS_v2_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_MEM_ALLOC_NODE_PARAMS_v2_st _pvt_val cdef cydriver.CUDA_MEM_ALLOC_NODE_PARAMS_v2_st* _pvt_ptr @@ -4664,6 +4776,7 @@ cdef class CUDA_MEM_FREE_NODE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_MEM_FREE_NODE_PARAMS_st _pvt_val cdef cydriver.CUDA_MEM_FREE_NODE_PARAMS_st* _pvt_ptr @@ -4694,6 +4807,7 @@ cdef class CUDA_CHILD_GRAPH_NODE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_CHILD_GRAPH_NODE_PARAMS_st _pvt_val cdef cydriver.CUDA_CHILD_GRAPH_NODE_PARAMS_st* _pvt_ptr @@ -4724,6 +4838,7 @@ cdef class CUDA_EVENT_RECORD_NODE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EVENT_RECORD_NODE_PARAMS_st* _val_ptr cdef cydriver.CUDA_EVENT_RECORD_NODE_PARAMS_st* _pvt_ptr @@ -4752,6 +4867,7 @@ cdef class CUDA_EVENT_WAIT_NODE_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUDA_EVENT_WAIT_NODE_PARAMS_st _pvt_val cdef cydriver.CUDA_EVENT_WAIT_NODE_PARAMS_st* _pvt_ptr @@ -4830,6 +4946,7 @@ cdef class CUgraphNodeParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUgraphNodeParams_st* _val_ptr cdef cydriver.CUgraphNodeParams_st* _pvt_ptr @@ -4898,6 +5015,7 @@ cdef class CUcheckpointCustomStoragePerDeviceData_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUcheckpointCustomStoragePerDeviceData_st _pvt_val cdef cydriver.CUcheckpointCustomStoragePerDeviceData_st* _pvt_ptr @@ -4933,6 +5051,7 @@ cdef class CUcheckpointCustomStorageInfo_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUcheckpointCustomStorageInfo_st _pvt_val cdef cydriver.CUcheckpointCustomStorageInfo_st* _pvt_ptr @@ -4960,6 +5079,7 @@ cdef class CUcheckpointLockArgs_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUcheckpointLockArgs_st _pvt_val cdef cydriver.CUcheckpointLockArgs_st* _pvt_ptr @@ -4980,6 +5100,7 @@ cdef class CUcheckpointCheckpointArgs_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUcheckpointCheckpointArgs_st _pvt_val cdef cydriver.CUcheckpointCheckpointArgs_st* _pvt_ptr @@ -5003,6 +5124,7 @@ cdef class CUcheckpointGpuPair_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUcheckpointGpuPair_st _pvt_val cdef cydriver.CUcheckpointGpuPair_st* _pvt_ptr @@ -5037,6 +5159,7 @@ cdef class CUcheckpointRestoreArgs_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUcheckpointRestoreArgs_st _pvt_val cdef cydriver.CUcheckpointRestoreArgs_st* _pvt_ptr @@ -5053,6 +5176,7 @@ cdef class CUcheckpointUnlockArgs_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUcheckpointUnlockArgs_st _pvt_val cdef cydriver.CUcheckpointUnlockArgs_st* _pvt_ptr @@ -5102,9 +5226,14 @@ cdef class CUmemDecompressParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUmemDecompressParams_st _pvt_val cdef cydriver.CUmemDecompressParams_st* _pvt_ptr + cdef size_t _dstActBytes_length + cdef cydriver.cuuint32_t* _dstActBytes + + cdef _HelperInputVoidPtr _cysrc @@ -5131,6 +5260,7 @@ cdef class CUcliqueInfo_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUcliqueInfo_st _pvt_val cdef cydriver.CUcliqueInfo_st* _pvt_ptr @@ -5150,6 +5280,7 @@ cdef class CUlogicalEndpointFabricHandle_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlogicalEndpointFabricHandle_st _pvt_val cdef cydriver.CUlogicalEndpointFabricHandle_st* _pvt_ptr @@ -5167,6 +5298,7 @@ cdef class anon_struct26: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlogicalEndpointProp_struct* _pvt_ptr cdef CUdevice _device @@ -5186,6 +5318,7 @@ cdef class anon_struct27: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlogicalEndpointProp_struct* _pvt_ptr cdef class CUlogicalEndpointProp_struct: @@ -5225,6 +5358,7 @@ cdef class CUlogicalEndpointProp_struct: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUlogicalEndpointProp_struct* _val_ptr cdef cydriver.CUlogicalEndpointProp_struct* _pvt_ptr @@ -5272,6 +5406,7 @@ cdef class CUdevSmResource_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUdevSmResource_st _pvt_val cdef cydriver.CUdevSmResource_st* _pvt_ptr @@ -5297,6 +5432,7 @@ cdef class CUdevWorkqueueConfigResource_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUdevWorkqueueConfigResource_st _pvt_val cdef cydriver.CUdevWorkqueueConfigResource_st* _pvt_ptr @@ -5310,6 +5446,7 @@ cdef class CUdevWorkqueueResource_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUdevWorkqueueResource_st _pvt_val cdef cydriver.CUdevWorkqueueResource_st* _pvt_ptr @@ -5347,6 +5484,7 @@ cdef class CU_DEV_SM_RESOURCE_GROUP_PARAMS_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CU_DEV_SM_RESOURCE_GROUP_PARAMS_st _pvt_val cdef cydriver.CU_DEV_SM_RESOURCE_GROUP_PARAMS_st* _pvt_ptr @@ -5390,6 +5528,7 @@ cdef class CUdevResource_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUdevResource_st* _val_ptr cdef cydriver.CUdevResource_st* _pvt_ptr @@ -5424,6 +5563,7 @@ cdef class anon_union21: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUeglFrame_st* _pvt_ptr cdef class CUeglFrame_st: @@ -5480,6 +5620,7 @@ cdef class CUeglFrame_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cydriver.CUeglFrame_st* _val_ptr cdef cydriver.CUeglFrame_st* _pvt_ptr diff --git a/cuda_bindings/cuda/bindings/driver.pyx b/cuda_bindings/cuda/bindings/driver.pyx index 4a3394ff3c6..c999fb467f4 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.4.1. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=a7b7178cfb0e794181ba423ee5165219e30af7a6bad68db5b20076f8c3bf49c6 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=09b7034a85e8350f14d2f4170ff1d2ecfd97fc292bfd920ee428dafc0e9ecf1e from typing import Any, Optional import cython import ctypes @@ -10042,19 +10042,10 @@ cdef class CUstreamMemOpWaitValueParams_st: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._address = CUdeviceptr(_ptr=&self._pvt_ptr[0].waitValue.address) - - self._value = cuuint32_t(_ptr=&self._pvt_ptr[0].waitValue.value) - - self._value64 = cuuint64_t(_ptr=&self._pvt_ptr[0].waitValue.value64) - - self._alias = CUdeviceptr(_ptr=&self._pvt_ptr[0].waitValue.alias) - def __dealloc__(self): pass def getPtr(self): @@ -10228,19 +10219,10 @@ cdef class CUstreamMemOpWriteValueParams_st: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._address = CUdeviceptr(_ptr=&self._pvt_ptr[0].writeValue.address) - - self._value = cuuint32_t(_ptr=&self._pvt_ptr[0].writeValue.value) - - self._value64 = cuuint64_t(_ptr=&self._pvt_ptr[0].writeValue.value64) - - self._alias = CUdeviceptr(_ptr=&self._pvt_ptr[0].writeValue.alias) - def __dealloc__(self): pass def getPtr(self): @@ -10542,16 +10524,9 @@ cdef class CUstreamMemOpAtomicReductionParams_st: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._address = CUdeviceptr(_ptr=&self._pvt_ptr[0].atomicReduction.address) - - self._value = cuuint64_t(_ptr=&self._pvt_ptr[0].atomicReduction.value) - - self._alias = CUdeviceptr(_ptr=&self._pvt_ptr[0].atomicReduction.alias) - def __dealloc__(self): pass def getPtr(self): @@ -10740,24 +10715,22 @@ cdef class CUstreamBatchMemOpParams_union: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._waitValue = CUstreamMemOpWaitValueParams_st(_ptr=self._pvt_ptr) - - + self._waitValue._owner = self self._writeValue = CUstreamMemOpWriteValueParams_st(_ptr=self._pvt_ptr) - - + self._writeValue._owner = self self._flushRemoteWrites = CUstreamMemOpFlushRemoteWritesParams_st(_ptr=self._pvt_ptr) - - + self._flushRemoteWrites._owner = self self._memoryBarrier = CUstreamMemOpMemoryBarrierParams_st(_ptr=self._pvt_ptr) - - + self._memoryBarrier._owner = self self._atomicReduction = CUstreamMemOpAtomicReductionParams_st(_ptr=self._pvt_ptr) - + self._atomicReduction._owner = self def __dealloc__(self): - pass + self._waitValue = None + self._writeValue = None + self._flushRemoteWrites = None + self._memoryBarrier = None + self._atomicReduction = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -10901,16 +10874,11 @@ cdef class CUDA_BATCH_MEM_OP_NODE_PARAMS_v1_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._ctx = CUcontext(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): - if self._paramArray is not NULL: free(self._paramArray) self._pvt_ptr[0].paramArray = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -10971,8 +10939,12 @@ cdef class CUDA_BATCH_MEM_OP_NODE_PARAMS_v1_st: @property def paramArray(self): - arrs = [self._pvt_ptr[0].paramArray + x*sizeof(cydriver.CUstreamBatchMemOpParams) for x in range(self._paramArray_length)] - return [CUstreamBatchMemOpParams(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].paramArray == NULL: + return [] + out_paramArray = [CUstreamBatchMemOpParams() for _idx in range(self._paramArray_length)] + for _idx in range(len(out_paramArray)): + string.memcpy(out_paramArray[_idx].getPtr(), &self._pvt_ptr[0].paramArray[_idx], sizeof(cydriver.CUstreamBatchMemOpParams)) + return out_paramArray @paramArray.setter def paramArray(self, val): cdef cydriver.CUstreamBatchMemOpParams* _paramArray_new @@ -10983,10 +10955,6 @@ cdef class CUDA_BATCH_MEM_OP_NODE_PARAMS_v1_st: self._pvt_ptr[0].paramArray = NULL else: if self._paramArray_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _paramArray_new = calloc(len(val), sizeof(cydriver.CUstreamBatchMemOpParams)) if _paramArray_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUstreamBatchMemOpParams))) @@ -11001,7 +10969,6 @@ cdef class CUDA_BATCH_MEM_OP_NODE_PARAMS_v1_st: string.memcpy(&self._paramArray[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUstreamBatchMemOpParams)) - @property def flags(self): return self._pvt_ptr[0].flags @@ -11044,16 +11011,11 @@ cdef class CUDA_BATCH_MEM_OP_NODE_PARAMS_v2_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._ctx = CUcontext(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): - if self._paramArray is not NULL: free(self._paramArray) self._pvt_ptr[0].paramArray = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -11114,8 +11076,12 @@ cdef class CUDA_BATCH_MEM_OP_NODE_PARAMS_v2_st: @property def paramArray(self): - arrs = [self._pvt_ptr[0].paramArray + x*sizeof(cydriver.CUstreamBatchMemOpParams) for x in range(self._paramArray_length)] - return [CUstreamBatchMemOpParams(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].paramArray == NULL: + return [] + out_paramArray = [CUstreamBatchMemOpParams() for _idx in range(self._paramArray_length)] + for _idx in range(len(out_paramArray)): + string.memcpy(out_paramArray[_idx].getPtr(), &self._pvt_ptr[0].paramArray[_idx], sizeof(cydriver.CUstreamBatchMemOpParams)) + return out_paramArray @paramArray.setter def paramArray(self, val): cdef cydriver.CUstreamBatchMemOpParams* _paramArray_new @@ -11126,10 +11092,6 @@ cdef class CUDA_BATCH_MEM_OP_NODE_PARAMS_v2_st: self._pvt_ptr[0].paramArray = NULL else: if self._paramArray_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _paramArray_new = calloc(len(val), sizeof(cydriver.CUstreamBatchMemOpParams)) if _paramArray_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUstreamBatchMemOpParams))) @@ -11144,7 +11106,6 @@ cdef class CUDA_BATCH_MEM_OP_NODE_PARAMS_v2_st: string.memcpy(&self._paramArray[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUstreamBatchMemOpParams)) - @property def flags(self): return self._pvt_ptr[0].flags @@ -11215,12 +11176,10 @@ cdef class anon_union2: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._overBudget = anon_struct0(_ptr=self._pvt_ptr) - + self._overBudget._owner = self def __dealloc__(self): - pass + self._overBudget = None def getPtr(self): return &self._pvt_ptr[0].info def __repr__(self): @@ -11272,11 +11231,10 @@ cdef class CUasyncNotificationInfo_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._info = anon_union2(_ptr=self._pvt_ptr) - + self._info._owner = self def __dealloc__(self): + self._info = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -11717,10 +11675,7 @@ cdef class CUDA_KERNEL_NODE_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._func = CUfunction(_ptr=&self._pvt_ptr[0].func) - def __dealloc__(self): pass def getPtr(self): @@ -11871,7 +11826,7 @@ cdef class CUDA_KERNEL_NODE_PARAMS_st: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams @property @@ -11950,16 +11905,9 @@ cdef class CUDA_KERNEL_NODE_PARAMS_v2_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._func = CUfunction(_ptr=&self._pvt_ptr[0].func) - - self._kern = CUkernel(_ptr=&self._pvt_ptr[0].kern) - - self._ctx = CUcontext(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): pass def getPtr(self): @@ -12122,7 +12070,7 @@ cdef class CUDA_KERNEL_NODE_PARAMS_v2_st: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams @property @@ -12235,16 +12183,9 @@ cdef class CUDA_KERNEL_NODE_PARAMS_v3_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._func = CUfunction(_ptr=&self._pvt_ptr[0].func) - - self._kern = CUkernel(_ptr=&self._pvt_ptr[0].kern) - - self._ctx = CUcontext(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): pass def getPtr(self): @@ -12407,7 +12348,7 @@ cdef class CUDA_KERNEL_NODE_PARAMS_v3_st: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams @property @@ -12494,10 +12435,7 @@ cdef class CUDA_MEMSET_NODE_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._dst = CUdeviceptr(_ptr=&self._pvt_ptr[0].dst) - def __dealloc__(self): pass def getPtr(self): @@ -12649,13 +12587,8 @@ cdef class CUDA_MEMSET_NODE_PARAMS_v2_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._dst = CUdeviceptr(_ptr=&self._pvt_ptr[0].dst) - - self._ctx = CUcontext(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): pass def getPtr(self): @@ -12810,10 +12743,7 @@ cdef class CUDA_HOST_NODE_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._fn = CUhostFn(_ptr=&self._pvt_ptr[0].fn) - def __dealloc__(self): pass def getPtr(self): @@ -12902,16 +12832,9 @@ cdef class CUDA_HOST_NODE_PARAMS_v2_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._fn = CUhostFn(_ptr=&self._pvt_ptr[0].fn) - - self._ctx = CUcontext(_ptr=&self._pvt_ptr[0].ctx) - - self._gCtx = CUgreenCtx(_ptr=&self._pvt_ptr[0].gCtx) - def __dealloc__(self): if self._val_ptr is not NULL: free(self._val_ptr) @@ -13079,13 +13002,8 @@ cdef class CUDA_CONDITIONAL_NODE_PARAMS: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._handle = CUgraphConditionalHandle(_ptr=&self._pvt_ptr[0].handle) - - self._ctx = CUcontext(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): pass def getPtr(self): @@ -13320,16 +13238,9 @@ cdef class CUDA_GRAPH_INSTANTIATE_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._flags = cuuint64_t(_ptr=&self._pvt_ptr[0].flags) - - self._hUploadStream = CUstream(_ptr=&self._pvt_ptr[0].hUploadStream) - - self._hErrNode_out = CUgraphNode(_ptr=&self._pvt_ptr[0].hErrNode_out) - def __dealloc__(self): pass def getPtr(self): @@ -13603,10 +13514,7 @@ cdef class anon_struct2: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._event = CUevent(_ptr=&self._pvt_ptr[0].programmaticEvent.event) - def __dealloc__(self): pass def getPtr(self): @@ -13691,10 +13599,7 @@ cdef class anon_struct3: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._event = CUevent(_ptr=&self._pvt_ptr[0].launchCompletionEvent.event) - def __dealloc__(self): pass def getPtr(self): @@ -13845,10 +13750,7 @@ cdef class anon_struct5: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._devNode = CUgraphDeviceNode(_ptr=&self._pvt_ptr[0].deviceUpdatableKernelNode.devNode) - def __dealloc__(self): pass def getPtr(self): @@ -14030,30 +13932,28 @@ cdef class CUlaunchAttributeValue_union: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._accessPolicyWindow = CUaccessPolicyWindow(_ptr=&self._pvt_ptr[0].accessPolicyWindow) - - + self._accessPolicyWindow._owner = self self._clusterDim = anon_struct1(_ptr=self._pvt_ptr) - - + self._clusterDim._owner = self self._programmaticEvent = anon_struct2(_ptr=self._pvt_ptr) - - + self._programmaticEvent._owner = self self._launchCompletionEvent = anon_struct3(_ptr=self._pvt_ptr) - - + self._launchCompletionEvent._owner = self self._memSyncDomainMap = CUlaunchMemSyncDomainMap(_ptr=&self._pvt_ptr[0].memSyncDomainMap) - - + self._memSyncDomainMap._owner = self self._preferredClusterDim = anon_struct4(_ptr=self._pvt_ptr) - - + self._preferredClusterDim._owner = self self._deviceUpdatableKernelNode = anon_struct5(_ptr=self._pvt_ptr) - + self._deviceUpdatableKernelNode._owner = self def __dealloc__(self): - pass + self._accessPolicyWindow = None + self._clusterDim = None + self._programmaticEvent = None + self._launchCompletionEvent = None + self._memSyncDomainMap = None + self._preferredClusterDim = None + self._deviceUpdatableKernelNode = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -14352,12 +14252,10 @@ cdef class CUlaunchAttribute_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._value = CUlaunchAttributeValue(_ptr=&self._pvt_ptr[0].value) - + self._value._owner = self def __dealloc__(self): - pass + self._value = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -14453,16 +14351,11 @@ cdef class CUlaunchConfig_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._hStream = CUstream(_ptr=&self._pvt_ptr[0].hStream) - def __dealloc__(self): - if self._attrs is not NULL: free(self._attrs) self._pvt_ptr[0].attrs = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -14607,8 +14500,12 @@ cdef class CUlaunchConfig_st: @property def attrs(self): - arrs = [self._pvt_ptr[0].attrs + x*sizeof(cydriver.CUlaunchAttribute) for x in range(self._attrs_length)] - return [CUlaunchAttribute(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].attrs == NULL: + return [] + out_attrs = [CUlaunchAttribute() for _idx in range(self._attrs_length)] + for _idx in range(len(out_attrs)): + string.memcpy(out_attrs[_idx].getPtr(), &self._pvt_ptr[0].attrs[_idx], sizeof(cydriver.CUlaunchAttribute)) + return out_attrs @attrs.setter def attrs(self, val): cdef cydriver.CUlaunchAttribute* _attrs_new @@ -14619,10 +14516,6 @@ cdef class CUlaunchConfig_st: self._pvt_ptr[0].attrs = NULL else: if self._attrs_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _attrs_new = calloc(len(val), sizeof(cydriver.CUlaunchAttribute)) if _attrs_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUlaunchAttribute))) @@ -14637,7 +14530,6 @@ cdef class CUlaunchConfig_st: string.memcpy(&self._attrs[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUlaunchAttribute)) - @property def numAttrs(self): return self._pvt_ptr[0].numAttrs @@ -14712,12 +14604,10 @@ cdef class anon_union4: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._smCount = CUexecAffinitySmCount(_ptr=&self._pvt_ptr[0].param.smCount) - + self._smCount._owner = self def __dealloc__(self): - pass + self._smCount = None def getPtr(self): return &self._pvt_ptr[0].param def __repr__(self): @@ -14768,11 +14658,10 @@ cdef class CUexecAffinityParam_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._param = anon_union4(_ptr=self._pvt_ptr) - + self._param._owner = self def __dealloc__(self): + self._param = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -14919,16 +14808,12 @@ cdef class CUctxCreateParams_st: def __init__(self, void_ptr _ptr = 0): pass def __dealloc__(self): - if self._execAffinityParams is not NULL: free(self._execAffinityParams) self._pvt_ptr[0].execAffinityParams = NULL - - if self._cigParams is not NULL: free(self._cigParams) self._pvt_ptr[0].cigParams = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -14958,8 +14843,12 @@ cdef class CUctxCreateParams_st: @property def execAffinityParams(self): - arrs = [self._pvt_ptr[0].execAffinityParams + x*sizeof(cydriver.CUexecAffinityParam) for x in range(self._execAffinityParams_length)] - return [CUexecAffinityParam(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].execAffinityParams == NULL: + return [] + out_execAffinityParams = [CUexecAffinityParam() for _idx in range(self._execAffinityParams_length)] + for _idx in range(len(out_execAffinityParams)): + string.memcpy(out_execAffinityParams[_idx].getPtr(), &self._pvt_ptr[0].execAffinityParams[_idx], sizeof(cydriver.CUexecAffinityParam)) + return out_execAffinityParams @execAffinityParams.setter def execAffinityParams(self, val): cdef cydriver.CUexecAffinityParam* _execAffinityParams_new @@ -14970,10 +14859,6 @@ cdef class CUctxCreateParams_st: self._pvt_ptr[0].execAffinityParams = NULL else: if self._execAffinityParams_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _execAffinityParams_new = calloc(len(val), sizeof(cydriver.CUexecAffinityParam)) if _execAffinityParams_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUexecAffinityParam))) @@ -14988,7 +14873,6 @@ cdef class CUctxCreateParams_st: string.memcpy(&self._execAffinityParams[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUexecAffinityParam)) - @property def numExecAffinityParams(self): return self._pvt_ptr[0].numExecAffinityParams @@ -14999,8 +14883,12 @@ cdef class CUctxCreateParams_st: @property def cigParams(self): - arrs = [self._pvt_ptr[0].cigParams + x*sizeof(cydriver.CUctxCigParam) for x in range(self._cigParams_length)] - return [CUctxCigParam(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].cigParams == NULL: + return [] + out_cigParams = [CUctxCigParam() for _idx in range(self._cigParams_length)] + for _idx in range(len(out_cigParams)): + string.memcpy(out_cigParams[_idx].getPtr(), &self._pvt_ptr[0].cigParams[_idx], sizeof(cydriver.CUctxCigParam)) + return out_cigParams @cigParams.setter def cigParams(self, val): cdef cydriver.CUctxCigParam* _cigParams_new @@ -15011,10 +14899,6 @@ cdef class CUctxCreateParams_st: self._pvt_ptr[0].cigParams = NULL else: if self._cigParams_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _cigParams_new = calloc(len(val), sizeof(cydriver.CUctxCigParam)) if _cigParams_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUctxCigParam))) @@ -15029,7 +14913,6 @@ cdef class CUctxCreateParams_st: string.memcpy(&self._cigParams[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUctxCigParam)) - cdef class CUstreamCigParam_st: """ CIG Stream Capture Params @@ -15124,11 +15007,9 @@ cdef class CUstreamCigCaptureParams_st: def __init__(self, void_ptr _ptr = 0): pass def __dealloc__(self): - if self._streamCigParams is not NULL: free(self._streamCigParams) self._pvt_ptr[0].streamCigParams = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -15146,8 +15027,12 @@ cdef class CUstreamCigCaptureParams_st: @property def streamCigParams(self): - arrs = [self._pvt_ptr[0].streamCigParams + x*sizeof(cydriver.CUstreamCigParam) for x in range(self._streamCigParams_length)] - return [CUstreamCigParam(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].streamCigParams == NULL: + return [] + out_streamCigParams = [CUstreamCigParam() for _idx in range(self._streamCigParams_length)] + for _idx in range(len(out_streamCigParams)): + string.memcpy(out_streamCigParams[_idx].getPtr(), &self._pvt_ptr[0].streamCigParams[_idx], sizeof(cydriver.CUstreamCigParam)) + return out_streamCigParams @streamCigParams.setter def streamCigParams(self, val): cdef cydriver.CUstreamCigParam* _streamCigParams_new @@ -15158,10 +15043,6 @@ cdef class CUstreamCigCaptureParams_st: self._pvt_ptr[0].streamCigParams = NULL else: if self._streamCigParams_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _streamCigParams_new = calloc(len(val), sizeof(cydriver.CUstreamCigParam)) if _streamCigParams_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUstreamCigParam))) @@ -15176,7 +15057,6 @@ cdef class CUstreamCigCaptureParams_st: string.memcpy(&self._streamCigParams[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUstreamCigParam)) - cdef class CUlibraryHostUniversalFunctionAndDataTable_st: """ Attributes @@ -15361,19 +15241,10 @@ cdef class CUDA_MEMCPY2D_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._srcDevice = CUdeviceptr(_ptr=&self._pvt_ptr[0].srcDevice) - - self._srcArray = CUarray(_ptr=&self._pvt_ptr[0].srcArray) - - self._dstDevice = CUdeviceptr(_ptr=&self._pvt_ptr[0].dstDevice) - - self._dstArray = CUarray(_ptr=&self._pvt_ptr[0].dstArray) - def __dealloc__(self): pass def getPtr(self): @@ -15760,19 +15631,10 @@ cdef class CUDA_MEMCPY3D_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._srcDevice = CUdeviceptr(_ptr=&self._pvt_ptr[0].srcDevice) - - self._srcArray = CUarray(_ptr=&self._pvt_ptr[0].srcArray) - - self._dstDevice = CUdeviceptr(_ptr=&self._pvt_ptr[0].dstDevice) - - self._dstArray = CUarray(_ptr=&self._pvt_ptr[0].dstArray) - def __dealloc__(self): pass def getPtr(self): @@ -16266,25 +16128,12 @@ cdef class CUDA_MEMCPY3D_PEER_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._srcDevice = CUdeviceptr(_ptr=&self._pvt_ptr[0].srcDevice) - - self._srcArray = CUarray(_ptr=&self._pvt_ptr[0].srcArray) - - self._srcContext = CUcontext(_ptr=&self._pvt_ptr[0].srcContext) - - self._dstDevice = CUdeviceptr(_ptr=&self._pvt_ptr[0].dstDevice) - - self._dstArray = CUarray(_ptr=&self._pvt_ptr[0].dstArray) - - self._dstContext = CUcontext(_ptr=&self._pvt_ptr[0].dstContext) - def __dealloc__(self): pass def getPtr(self): @@ -16734,15 +16583,11 @@ cdef class CUDA_MEMCPY_NODE_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._copyCtx = CUcontext(_ptr=&self._pvt_ptr[0].copyCtx) - - self._copyParams = CUDA_MEMCPY3D(_ptr=&self._pvt_ptr[0].copyParams) - + self._copyParams._owner = self def __dealloc__(self): - pass + self._copyParams = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -17158,12 +17003,10 @@ cdef class CUDA_ARRAY_SPARSE_PROPERTIES_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._tileExtent = anon_struct6(_ptr=self._pvt_ptr) - + self._tileExtent._owner = self def __dealloc__(self): - pass + self._tileExtent = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -17313,10 +17156,7 @@ cdef class anon_struct7: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._hArray = CUarray(_ptr=&self._pvt_ptr[0].res.array.hArray) - def __dealloc__(self): pass def getPtr(self): @@ -17369,10 +17209,7 @@ cdef class anon_struct8: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._hMipmappedArray = CUmipmappedArray(_ptr=&self._pvt_ptr[0].res.mipmap.hMipmappedArray) - def __dealloc__(self): pass def getPtr(self): @@ -17437,10 +17274,7 @@ cdef class anon_struct9: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._devPtr = CUdeviceptr(_ptr=&self._pvt_ptr[0].res.linear.devPtr) - def __dealloc__(self): pass def getPtr(self): @@ -17556,10 +17390,7 @@ cdef class anon_struct10: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._devPtr = CUdeviceptr(_ptr=&self._pvt_ptr[0].res.pitch2D.devPtr) - def __dealloc__(self): pass def getPtr(self): @@ -17719,21 +17550,19 @@ cdef class anon_union5: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._array = anon_struct7(_ptr=self._pvt_ptr) - - + self._array._owner = self self._mipmap = anon_struct8(_ptr=self._pvt_ptr) - - + self._mipmap._owner = self self._linear = anon_struct9(_ptr=self._pvt_ptr) - - + self._linear._owner = self self._pitch2D = anon_struct10(_ptr=self._pvt_ptr) - + self._pitch2D._owner = self def __dealloc__(self): - pass + self._array = None + self._mipmap = None + self._linear = None + self._pitch2D = None def getPtr(self): return &self._pvt_ptr[0].res def __repr__(self): @@ -17830,11 +17659,10 @@ cdef class CUDA_RESOURCE_DESC_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._res = anon_union5(_ptr=self._pvt_ptr) - + self._res._owner = self def __dealloc__(self): + self._res = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -18428,13 +18256,8 @@ cdef class CUDA_LAUNCH_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._function = CUfunction(_ptr=&self._pvt_ptr[0].function) - - self._hStream = CUstream(_ptr=&self._pvt_ptr[0].hStream) - def __dealloc__(self): pass def getPtr(self): @@ -18602,7 +18425,7 @@ cdef class CUDA_LAUNCH_PARAMS_st: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams cdef class anon_struct12: @@ -18695,12 +18518,10 @@ cdef class anon_union6: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._win32 = anon_struct12(_ptr=self._pvt_ptr) - + self._win32._owner = self def __dealloc__(self): - pass + self._win32 = None def getPtr(self): return &self._pvt_ptr[0].handle def __repr__(self): @@ -18788,11 +18609,10 @@ cdef class CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._handle = anon_union6(_ptr=self._pvt_ptr) - + self._handle._owner = self def __dealloc__(self): + self._handle = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -18975,12 +18795,10 @@ cdef class CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._arrayDesc = CUDA_ARRAY3D_DESCRIPTOR(_ptr=&self._pvt_ptr[0].arrayDesc) - + self._arrayDesc._owner = self def __dealloc__(self): - pass + self._arrayDesc = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -19122,12 +18940,10 @@ cdef class anon_union7: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._win32 = anon_struct13(_ptr=self._pvt_ptr) - + self._win32._owner = self def __dealloc__(self): - pass + self._win32 = None def getPtr(self): return &self._pvt_ptr[0].handle def __repr__(self): @@ -19211,11 +19027,10 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._handle = anon_union7(_ptr=self._pvt_ptr) - + self._handle._owner = self def __dealloc__(self): + self._handle = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -19428,18 +19243,16 @@ cdef class anon_struct16: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._fence = anon_struct14(_ptr=self._pvt_ptr) - - + self._fence._owner = self self._nvSciSync = anon_union8(_ptr=self._pvt_ptr) - - + self._nvSciSync._owner = self self._keyedMutex = anon_struct15(_ptr=self._pvt_ptr) - + self._keyedMutex._owner = self def __dealloc__(self): - pass + self._fence = None + self._nvSciSync = None + self._keyedMutex = None def getPtr(self): return &self._pvt_ptr[0].params def __repr__(self): @@ -19524,12 +19337,10 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._params = anon_struct16(_ptr=self._pvt_ptr) - + self._params._owner = self def __dealloc__(self): - pass + self._params = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -19744,18 +19555,16 @@ cdef class anon_struct19: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._fence = anon_struct17(_ptr=self._pvt_ptr) - - + self._fence._owner = self self._nvSciSync = anon_union9(_ptr=self._pvt_ptr) - - + self._nvSciSync._owner = self self._keyedMutex = anon_struct18(_ptr=self._pvt_ptr) - + self._keyedMutex._owner = self def __dealloc__(self): - pass + self._fence = None + self._nvSciSync = None + self._keyedMutex = None def getPtr(self): return &self._pvt_ptr[0].params def __repr__(self): @@ -19840,12 +19649,10 @@ cdef class CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._params = anon_struct19(_ptr=self._pvt_ptr) - + self._params._owner = self def __dealloc__(self): - pass + self._params = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -19916,16 +19723,12 @@ cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st: def __init__(self, void_ptr _ptr = 0): pass def __dealloc__(self): - if self._extSemArray is not NULL: free(self._extSemArray) self._pvt_ptr[0].extSemArray = NULL - - if self._paramsArray is not NULL: free(self._paramsArray) self._pvt_ptr[0].paramsArray = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -19979,8 +19782,12 @@ cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st: @property def paramsArray(self): - arrs = [self._pvt_ptr[0].paramsArray + x*sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS) for x in range(self._paramsArray_length)] - return [CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].paramsArray == NULL: + return [] + out_paramsArray = [CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS() for _idx in range(self._paramsArray_length)] + for _idx in range(len(out_paramsArray)): + string.memcpy(out_paramsArray[_idx].getPtr(), &self._pvt_ptr[0].paramsArray[_idx], sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS)) + return out_paramsArray @paramsArray.setter def paramsArray(self, val): cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* _paramsArray_new @@ -19991,10 +19798,6 @@ cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st: self._pvt_ptr[0].paramsArray = NULL else: if self._paramsArray_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _paramsArray_new = calloc(len(val), sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS)) if _paramsArray_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS))) @@ -20009,7 +19812,6 @@ cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st: string.memcpy(&self._paramsArray[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS)) - @property def numExtSems(self): return self._pvt_ptr[0].numExtSems @@ -20058,24 +19860,15 @@ cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._ctx = CUcontext(_ptr=&self._pvt_ptr[0].ctx) - - self._gCtx = CUgreenCtx(_ptr=&self._pvt_ptr[0].gCtx) - def __dealloc__(self): - if self._extSemArray is not NULL: free(self._extSemArray) self._pvt_ptr[0].extSemArray = NULL - - if self._paramsArray is not NULL: free(self._paramsArray) self._pvt_ptr[0].paramsArray = NULL - if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -20143,8 +19936,12 @@ cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2_st: @property def paramsArray(self): - arrs = [self._pvt_ptr[0].paramsArray + x*sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS) for x in range(self._paramsArray_length)] - return [CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].paramsArray == NULL: + return [] + out_paramsArray = [CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS() for _idx in range(self._paramsArray_length)] + for _idx in range(len(out_paramsArray)): + string.memcpy(out_paramsArray[_idx].getPtr(), &self._pvt_ptr[0].paramsArray[_idx], sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS)) + return out_paramsArray @paramsArray.setter def paramsArray(self, val): cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS* _paramsArray_new @@ -20155,10 +19952,6 @@ cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2_st: self._pvt_ptr[0].paramsArray = NULL else: if self._paramsArray_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _paramsArray_new = calloc(len(val), sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS)) if _paramsArray_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS))) @@ -20173,7 +19966,6 @@ cdef class CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2_st: string.memcpy(&self._paramsArray[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS)) - @property def numExtSems(self): return self._pvt_ptr[0].numExtSems @@ -20249,16 +20041,12 @@ cdef class CUDA_EXT_SEM_WAIT_NODE_PARAMS_st: def __init__(self, void_ptr _ptr = 0): pass def __dealloc__(self): - if self._extSemArray is not NULL: free(self._extSemArray) self._pvt_ptr[0].extSemArray = NULL - - if self._paramsArray is not NULL: free(self._paramsArray) self._pvt_ptr[0].paramsArray = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -20312,8 +20100,12 @@ cdef class CUDA_EXT_SEM_WAIT_NODE_PARAMS_st: @property def paramsArray(self): - arrs = [self._pvt_ptr[0].paramsArray + x*sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS) for x in range(self._paramsArray_length)] - return [CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].paramsArray == NULL: + return [] + out_paramsArray = [CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS() for _idx in range(self._paramsArray_length)] + for _idx in range(len(out_paramsArray)): + string.memcpy(out_paramsArray[_idx].getPtr(), &self._pvt_ptr[0].paramsArray[_idx], sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS)) + return out_paramsArray @paramsArray.setter def paramsArray(self, val): cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* _paramsArray_new @@ -20324,10 +20116,6 @@ cdef class CUDA_EXT_SEM_WAIT_NODE_PARAMS_st: self._pvt_ptr[0].paramsArray = NULL else: if self._paramsArray_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _paramsArray_new = calloc(len(val), sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS)) if _paramsArray_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS))) @@ -20342,7 +20130,6 @@ cdef class CUDA_EXT_SEM_WAIT_NODE_PARAMS_st: string.memcpy(&self._paramsArray[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS)) - @property def numExtSems(self): return self._pvt_ptr[0].numExtSems @@ -20391,24 +20178,15 @@ cdef class CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._ctx = CUcontext(_ptr=&self._pvt_ptr[0].ctx) - - self._gCtx = CUgreenCtx(_ptr=&self._pvt_ptr[0].gCtx) - def __dealloc__(self): - if self._extSemArray is not NULL: free(self._extSemArray) self._pvt_ptr[0].extSemArray = NULL - - if self._paramsArray is not NULL: free(self._paramsArray) self._pvt_ptr[0].paramsArray = NULL - if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -20476,8 +20254,12 @@ cdef class CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2_st: @property def paramsArray(self): - arrs = [self._pvt_ptr[0].paramsArray + x*sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS) for x in range(self._paramsArray_length)] - return [CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].paramsArray == NULL: + return [] + out_paramsArray = [CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS() for _idx in range(self._paramsArray_length)] + for _idx in range(len(out_paramsArray)): + string.memcpy(out_paramsArray[_idx].getPtr(), &self._pvt_ptr[0].paramsArray[_idx], sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS)) + return out_paramsArray @paramsArray.setter def paramsArray(self, val): cdef cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS* _paramsArray_new @@ -20488,10 +20270,6 @@ cdef class CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2_st: self._pvt_ptr[0].paramsArray = NULL else: if self._paramsArray_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _paramsArray_new = calloc(len(val), sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS)) if _paramsArray_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS))) @@ -20506,7 +20284,6 @@ cdef class CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2_st: string.memcpy(&self._paramsArray[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS)) - @property def numExtSems(self): return self._pvt_ptr[0].numExtSems @@ -20571,13 +20348,8 @@ cdef class anon_union12: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._mipmap = CUmipmappedArray(_ptr=&self._pvt_ptr[0].resource.mipmap) - - self._array = CUarray(_ptr=&self._pvt_ptr[0].resource.array) - def __dealloc__(self): pass def getPtr(self): @@ -20907,15 +20679,13 @@ cdef class anon_union13: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._sparseLevel = anon_struct20(_ptr=self._pvt_ptr) - - + self._sparseLevel._owner = self self._miptail = anon_struct21(_ptr=self._pvt_ptr) - + self._miptail._owner = self def __dealloc__(self): - pass + self._sparseLevel = None + self._miptail = None def getPtr(self): return &self._pvt_ptr[0].subresource def __repr__(self): @@ -20971,10 +20741,7 @@ cdef class anon_union14: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._memHandle = CUmemGenericAllocationHandle(_ptr=&self._pvt_ptr[0].memHandle.memHandle) - def __dealloc__(self): pass def getPtr(self): @@ -21070,17 +20837,16 @@ cdef class CUarrayMapInfo_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._resource = anon_union12(_ptr=self._pvt_ptr) - - + self._resource._owner = self self._subresource = anon_union13(_ptr=self._pvt_ptr) - - + self._subresource._owner = self self._memHandle = anon_union14(_ptr=self._pvt_ptr) - + self._memHandle._owner = self def __dealloc__(self): + self._resource = None + self._subresource = None + self._memHandle = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -21328,11 +21094,10 @@ cdef class CUmemLocation_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._localized = anon_struct22(_ptr=self._pvt_ptr) - + self._localized._owner = self def __dealloc__(self): + self._localized = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -21508,15 +21273,13 @@ cdef class CUmemAllocationProp_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._location = CUmemLocation(_ptr=&self._pvt_ptr[0].location) - - + self._location._owner = self self._allocFlags = anon_struct23(_ptr=self._pvt_ptr) - + self._allocFlags._owner = self def __dealloc__(self): - pass + self._location = None + self._allocFlags = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -21728,12 +21491,10 @@ cdef class CUmemAccessDesc_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._location = CUmemLocation(_ptr=&self._pvt_ptr[0].location) - + self._location._owner = self def __dealloc__(self): - pass + self._location = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -21804,13 +21565,8 @@ cdef class CUgraphExecUpdateResultInfo_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._errorNode = CUgraphNode(_ptr=&self._pvt_ptr[0].errorNode) - - self._errorFromNode = CUgraphNode(_ptr=&self._pvt_ptr[0].errorFromNode) - def __dealloc__(self): pass def getPtr(self): @@ -21948,12 +21704,10 @@ cdef class CUmemPoolProps_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._location = CUmemLocation(_ptr=&self._pvt_ptr[0].location) - + self._location._owner = self def __dealloc__(self): - pass + self._location = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -22128,15 +21882,13 @@ cdef class CUmemcpyAttributes_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._srcLocHint = CUmemLocation(_ptr=&self._pvt_ptr[0].srcLocHint) - - + self._srcLocHint._owner = self self._dstLocHint = CUmemLocation(_ptr=&self._pvt_ptr[0].dstLocHint) - + self._dstLocHint._owner = self def __dealloc__(self): - pass + self._srcLocHint = None + self._dstLocHint = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -22400,15 +22152,11 @@ cdef class anon_struct24: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._ptr = CUdeviceptr(_ptr=&self._pvt_ptr[0].op.ptr.ptr) - - self._locHint = CUmemLocation(_ptr=&self._pvt_ptr[0].op.ptr.locHint) - + self._locHint._owner = self def __dealloc__(self): - pass + self._locHint = None def getPtr(self): return &self._pvt_ptr[0].op.ptr def __repr__(self): @@ -22506,15 +22254,11 @@ cdef class anon_struct25: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._array = CUarray(_ptr=&self._pvt_ptr[0].op.array.array) - - self._offset = CUoffset3D(_ptr=&self._pvt_ptr[0].op.array.offset) - + self._offset._owner = self def __dealloc__(self): - pass + self._offset = None def getPtr(self): return &self._pvt_ptr[0].op.array def __repr__(self): @@ -22583,15 +22327,13 @@ cdef class anon_union16: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._ptr = anon_struct24(_ptr=self._pvt_ptr) - - + self._ptr._owner = self self._array = anon_struct25(_ptr=self._pvt_ptr) - + self._array._owner = self def __dealloc__(self): - pass + self._ptr = None + self._array = None def getPtr(self): return &self._pvt_ptr[0].op def __repr__(self): @@ -22656,11 +22398,10 @@ cdef class CUmemcpy3DOperand_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._op = anon_union16(_ptr=self._pvt_ptr) - + self._op._owner = self def __dealloc__(self): + self._op = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -22737,18 +22478,16 @@ cdef class CUDA_MEMCPY3D_BATCH_OP_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._src = CUmemcpy3DOperand(_ptr=&self._pvt_ptr[0].src) - - + self._src._owner = self self._dst = CUmemcpy3DOperand(_ptr=&self._pvt_ptr[0].dst) - - + self._dst._owner = self self._extent = CUextent3D(_ptr=&self._pvt_ptr[0].extent) - + self._extent._owner = self def __dealloc__(self): - pass + self._src = None + self._dst = None + self._extent = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -22870,19 +22609,14 @@ cdef class CUDA_MEM_ALLOC_NODE_PARAMS_v1_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._poolProps = CUmemPoolProps(_ptr=&self._pvt_ptr[0].poolProps) - - + self._poolProps._owner = self self._dptr = CUdeviceptr(_ptr=&self._pvt_ptr[0].dptr) - def __dealloc__(self): - + self._poolProps = None if self._accessDescs is not NULL: free(self._accessDescs) self._pvt_ptr[0].accessDescs = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -22932,8 +22666,12 @@ cdef class CUDA_MEM_ALLOC_NODE_PARAMS_v1_st: @property def accessDescs(self): - arrs = [self._pvt_ptr[0].accessDescs + x*sizeof(cydriver.CUmemAccessDesc) for x in range(self._accessDescs_length)] - return [CUmemAccessDesc(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].accessDescs == NULL: + return [] + out_accessDescs = [CUmemAccessDesc() for _idx in range(self._accessDescs_length)] + for _idx in range(len(out_accessDescs)): + string.memcpy(out_accessDescs[_idx].getPtr(), &self._pvt_ptr[0].accessDescs[_idx], sizeof(cydriver.CUmemAccessDesc)) + return out_accessDescs @accessDescs.setter def accessDescs(self, val): cdef cydriver.CUmemAccessDesc* _accessDescs_new @@ -22944,10 +22682,6 @@ cdef class CUDA_MEM_ALLOC_NODE_PARAMS_v1_st: self._pvt_ptr[0].accessDescs = NULL else: if self._accessDescs_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _accessDescs_new = calloc(len(val), sizeof(cydriver.CUmemAccessDesc)) if _accessDescs_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUmemAccessDesc))) @@ -22962,7 +22696,6 @@ cdef class CUDA_MEM_ALLOC_NODE_PARAMS_v1_st: string.memcpy(&self._accessDescs[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUmemAccessDesc)) - @property def accessDescCount(self): return self._pvt_ptr[0].accessDescCount @@ -23039,19 +22772,14 @@ cdef class CUDA_MEM_ALLOC_NODE_PARAMS_v2_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._poolProps = CUmemPoolProps(_ptr=&self._pvt_ptr[0].poolProps) - - + self._poolProps._owner = self self._dptr = CUdeviceptr(_ptr=&self._pvt_ptr[0].dptr) - def __dealloc__(self): - + self._poolProps = None if self._accessDescs is not NULL: free(self._accessDescs) self._pvt_ptr[0].accessDescs = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -23101,8 +22829,12 @@ cdef class CUDA_MEM_ALLOC_NODE_PARAMS_v2_st: @property def accessDescs(self): - arrs = [self._pvt_ptr[0].accessDescs + x*sizeof(cydriver.CUmemAccessDesc) for x in range(self._accessDescs_length)] - return [CUmemAccessDesc(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].accessDescs == NULL: + return [] + out_accessDescs = [CUmemAccessDesc() for _idx in range(self._accessDescs_length)] + for _idx in range(len(out_accessDescs)): + string.memcpy(out_accessDescs[_idx].getPtr(), &self._pvt_ptr[0].accessDescs[_idx], sizeof(cydriver.CUmemAccessDesc)) + return out_accessDescs @accessDescs.setter def accessDescs(self, val): cdef cydriver.CUmemAccessDesc* _accessDescs_new @@ -23113,10 +22845,6 @@ cdef class CUDA_MEM_ALLOC_NODE_PARAMS_v2_st: self._pvt_ptr[0].accessDescs = NULL else: if self._accessDescs_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _accessDescs_new = calloc(len(val), sizeof(cydriver.CUmemAccessDesc)) if _accessDescs_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUmemAccessDesc))) @@ -23131,7 +22859,6 @@ cdef class CUDA_MEM_ALLOC_NODE_PARAMS_v2_st: string.memcpy(&self._accessDescs[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUmemAccessDesc)) - @property def accessDescCount(self): return self._pvt_ptr[0].accessDescCount @@ -23188,10 +22915,7 @@ cdef class CUDA_MEM_FREE_NODE_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._dptr = CUdeviceptr(_ptr=&self._pvt_ptr[0].dptr) - def __dealloc__(self): pass def getPtr(self): @@ -23257,10 +22981,7 @@ cdef class CUDA_CHILD_GRAPH_NODE_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._graph = CUgraph(_ptr=&self._pvt_ptr[0].graph) - def __dealloc__(self): pass def getPtr(self): @@ -23340,16 +23061,9 @@ cdef class CUDA_EVENT_RECORD_NODE_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._event = CUevent(_ptr=&self._pvt_ptr[0].event) - - self._ctx = CUcontext(_ptr=&self._pvt_ptr[0].ctx) - - self._gCtx = CUgreenCtx(_ptr=&self._pvt_ptr[0].gCtx) - def __dealloc__(self): if self._val_ptr is not NULL: free(self._val_ptr) @@ -23453,10 +23167,7 @@ cdef class CUDA_EVENT_WAIT_NODE_PARAMS_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._event = CUevent(_ptr=&self._pvt_ptr[0].event) - def __dealloc__(self): pass def getPtr(self): @@ -23570,47 +23281,46 @@ cdef class CUgraphNodeParams_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._kernel = CUDA_KERNEL_NODE_PARAMS_v3(_ptr=&self._pvt_ptr[0].kernel) - - + self._kernel._owner = self self._memcpy = CUDA_MEMCPY_NODE_PARAMS(_ptr=&self._pvt_ptr[0].memcpy) - - + self._memcpy._owner = self self._memset = CUDA_MEMSET_NODE_PARAMS_v2(_ptr=&self._pvt_ptr[0].memset) - - + self._memset._owner = self self._host = CUDA_HOST_NODE_PARAMS_v2(_ptr=&self._pvt_ptr[0].host) - - + self._host._owner = self self._graph = CUDA_CHILD_GRAPH_NODE_PARAMS(_ptr=&self._pvt_ptr[0].graph) - - + self._graph._owner = self self._eventWait = CUDA_EVENT_WAIT_NODE_PARAMS(_ptr=&self._pvt_ptr[0].eventWait) - - + self._eventWait._owner = self self._eventRecord = CUDA_EVENT_RECORD_NODE_PARAMS(_ptr=&self._pvt_ptr[0].eventRecord) - - + self._eventRecord._owner = self self._extSemSignal = CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2(_ptr=&self._pvt_ptr[0].extSemSignal) - - + self._extSemSignal._owner = self self._extSemWait = CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2(_ptr=&self._pvt_ptr[0].extSemWait) - - + self._extSemWait._owner = self self._alloc = CUDA_MEM_ALLOC_NODE_PARAMS_v2(_ptr=&self._pvt_ptr[0].alloc) - - + self._alloc._owner = self self._free = CUDA_MEM_FREE_NODE_PARAMS(_ptr=&self._pvt_ptr[0].free) - - + self._free._owner = self self._memOp = CUDA_BATCH_MEM_OP_NODE_PARAMS_v2(_ptr=&self._pvt_ptr[0].memOp) - - + self._memOp._owner = self self._conditional = CUDA_CONDITIONAL_NODE_PARAMS(_ptr=&self._pvt_ptr[0].conditional) - + self._conditional._owner = self def __dealloc__(self): + self._kernel = None + self._memcpy = None + self._memset = None + self._host = None + self._graph = None + self._eventWait = None + self._eventRecord = None + self._extSemSignal = None + self._extSemWait = None + self._alloc = None + self._free = None + self._memOp = None + self._conditional = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -23875,13 +23585,8 @@ cdef class CUcheckpointCustomStoragePerDeviceData_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._devPtr = CUdeviceptr(_ptr=&self._pvt_ptr[0].devPtr) - - self._stream = CUstream(_ptr=&self._pvt_ptr[0].stream) - def __dealloc__(self): pass def getPtr(self): @@ -23986,16 +23691,11 @@ cdef class CUcheckpointCustomStorageInfo_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._handle = CUcheckpointOperationHandle(_ptr=&self._pvt_ptr[0].handle) - def __dealloc__(self): - if self._perDeviceData is not NULL: free(self._perDeviceData) self._pvt_ptr[0].perDeviceData = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -24042,8 +23742,12 @@ cdef class CUcheckpointCustomStorageInfo_st: @property def perDeviceData(self): - arrs = [self._pvt_ptr[0].perDeviceData + x*sizeof(cydriver.CUcheckpointCustomStoragePerDeviceData) for x in range(self._perDeviceData_length)] - return [CUcheckpointCustomStoragePerDeviceData(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].perDeviceData == NULL: + return [] + out_perDeviceData = [CUcheckpointCustomStoragePerDeviceData() for _idx in range(self._perDeviceData_length)] + for _idx in range(len(out_perDeviceData)): + string.memcpy(out_perDeviceData[_idx].getPtr(), &self._pvt_ptr[0].perDeviceData[_idx], sizeof(cydriver.CUcheckpointCustomStoragePerDeviceData)) + return out_perDeviceData @perDeviceData.setter def perDeviceData(self, val): cdef cydriver.CUcheckpointCustomStoragePerDeviceData* _perDeviceData_new @@ -24054,10 +23758,6 @@ cdef class CUcheckpointCustomStorageInfo_st: self._pvt_ptr[0].perDeviceData = NULL else: if self._perDeviceData_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _perDeviceData_new = calloc(len(val), sizeof(cydriver.CUcheckpointCustomStoragePerDeviceData)) if _perDeviceData_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUcheckpointCustomStoragePerDeviceData))) @@ -24072,7 +23772,6 @@ cdef class CUcheckpointCustomStorageInfo_st: string.memcpy(&self._perDeviceData[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUcheckpointCustomStoragePerDeviceData)) - @property def deviceCount(self): return self._pvt_ptr[0].deviceCount @@ -24205,15 +23904,13 @@ cdef class CUcheckpointGpuPair_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._oldUuid = CUuuid(_ptr=&self._pvt_ptr[0].oldUuid) - - + self._oldUuid._owner = self self._newUuid = CUuuid(_ptr=&self._pvt_ptr[0].newUuid) - + self._newUuid._owner = self def __dealloc__(self): - pass + self._oldUuid = None + self._newUuid = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -24284,11 +23981,9 @@ cdef class CUcheckpointRestoreArgs_st: def __init__(self, void_ptr _ptr = 0): pass def __dealloc__(self): - if self._gpuPairs is not NULL: free(self._gpuPairs) self._pvt_ptr[0].gpuPairs = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -24318,8 +24013,12 @@ cdef class CUcheckpointRestoreArgs_st: @property def gpuPairs(self): - arrs = [self._pvt_ptr[0].gpuPairs + x*sizeof(cydriver.CUcheckpointGpuPair) for x in range(self._gpuPairs_length)] - return [CUcheckpointGpuPair(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].gpuPairs == NULL: + return [] + out_gpuPairs = [CUcheckpointGpuPair() for _idx in range(self._gpuPairs_length)] + for _idx in range(len(out_gpuPairs)): + string.memcpy(out_gpuPairs[_idx].getPtr(), &self._pvt_ptr[0].gpuPairs[_idx], sizeof(cydriver.CUcheckpointGpuPair)) + return out_gpuPairs @gpuPairs.setter def gpuPairs(self, val): cdef cydriver.CUcheckpointGpuPair* _gpuPairs_new @@ -24330,10 +24029,6 @@ cdef class CUcheckpointRestoreArgs_st: self._pvt_ptr[0].gpuPairs = NULL else: if self._gpuPairs_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _gpuPairs_new = calloc(len(val), sizeof(cydriver.CUcheckpointGpuPair)) if _gpuPairs_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUcheckpointGpuPair))) @@ -24348,7 +24043,6 @@ cdef class CUcheckpointRestoreArgs_st: string.memcpy(&self._gpuPairs[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUcheckpointGpuPair)) - @property def gpuPairsCount(self): return self._pvt_ptr[0].gpuPairsCount @@ -24675,10 +24369,7 @@ cdef class anon_struct26: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._device = CUdevice(_ptr=&self._pvt_ptr[0].unicast.device) - def __dealloc__(self): pass def getPtr(self): @@ -24802,14 +24493,13 @@ cdef class CUlogicalEndpointProp_struct: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._unicast = anon_struct26(_ptr=self._pvt_ptr) - - + self._unicast._owner = self self._multicast = anon_struct27(_ptr=self._pvt_ptr) - + self._multicast._owner = self def __dealloc__(self): + self._unicast = None + self._multicast = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -25059,10 +24749,7 @@ cdef class CUdevWorkqueueConfigResource_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._device = CUdevice(_ptr=&self._pvt_ptr[0].device) - def __dealloc__(self): pass def getPtr(self): @@ -25321,22 +25008,19 @@ cdef class CUdevResource_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._sm = CUdevSmResource(_ptr=&self._pvt_ptr[0].sm) - - + self._sm._owner = self self._wqConfig = CUdevWorkqueueConfigResource(_ptr=&self._pvt_ptr[0].wqConfig) - - + self._wqConfig._owner = self self._wq = CUdevWorkqueueResource(_ptr=&self._pvt_ptr[0].wq) - + self._wq._owner = self def __dealloc__(self): - + self._sm = None + self._wqConfig = None + self._wq = None if self._nextResource is not NULL: free(self._nextResource) self._pvt_ptr[0].nextResource = NULL - if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -25446,8 +25130,12 @@ cdef class CUdevResource_st: @property def nextResource(self): - arrs = [self._pvt_ptr[0].nextResource + x*sizeof(cydriver.CUdevResource_st) for x in range(self._nextResource_length)] - return [CUdevResource_st(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].nextResource == NULL: + return [] + out_nextResource = [CUdevResource_st() for _idx in range(self._nextResource_length)] + for _idx in range(len(out_nextResource)): + string.memcpy(out_nextResource[_idx].getPtr(), &self._pvt_ptr[0].nextResource[_idx], sizeof(cydriver.CUdevResource_st)) + return out_nextResource @nextResource.setter def nextResource(self, val): cdef cydriver.CUdevResource_st* _nextResource_new @@ -25458,10 +25146,6 @@ cdef class CUdevResource_st: self._pvt_ptr[0].nextResource = NULL else: if self._nextResource_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _nextResource_new = calloc(len(val), sizeof(cydriver.CUdevResource_st)) if _nextResource_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cydriver.CUdevResource_st))) @@ -25476,7 +25160,6 @@ cdef class CUdevResource_st: string.memcpy(&self._nextResource[idx], (val[idx])._pvt_ptr, sizeof(cydriver.CUdevResource_st)) - cdef class anon_union21: """ Attributes @@ -25609,11 +25292,10 @@ cdef class CUeglFrame_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._frame = anon_union21(_ptr=self._pvt_ptr) - + self._frame._owner = self def __dealloc__(self): + self._frame = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -43780,7 +43462,7 @@ def cuLaunchKernel(f, unsigned int gridDimX, unsigned int gridDimY, unsigned int pf = int(CUfunction(f)) cyf = pf cdef _HelperKernelParams cykernelParams = _HelperKernelParams(kernelParams) - cdef void** cykernelParams_ptr = cykernelParams.ckernelParams + cdef void** cykernelParams_ptr = cykernelParams.ckernelParams with nogil: err = cydriver.cuLaunchKernel(cyf, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, cyhStream, cykernelParams_ptr, extra) return (_CUresult(err),) @@ -44018,7 +43700,7 @@ def cuLaunchKernelEx(config : Optional[CUlaunchConfig], f, kernelParams, void_pt cyf = pf cdef cydriver.CUlaunchConfig* cyconfig_ptr = config._pvt_ptr if config is not None else NULL cdef _HelperKernelParams cykernelParams = _HelperKernelParams(kernelParams) - cdef void** cykernelParams_ptr = cykernelParams.ckernelParams + cdef void** cykernelParams_ptr = cykernelParams.ckernelParams with nogil: err = cydriver.cuLaunchKernelEx(cyconfig_ptr, cyf, cykernelParams_ptr, extra) return (_CUresult(err),) @@ -44128,7 +43810,7 @@ def cuLaunchCooperativeKernel(f, unsigned int gridDimX, unsigned int gridDimY, u pf = int(CUfunction(f)) cyf = pf cdef _HelperKernelParams cykernelParams = _HelperKernelParams(kernelParams) - cdef void** cykernelParams_ptr = cykernelParams.ckernelParams + cdef void** cykernelParams_ptr = cykernelParams.ckernelParams with nogil: err = cydriver.cuLaunchCooperativeKernel(cyf, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, cyhStream, cykernelParams_ptr) return (_CUresult(err),) diff --git a/cuda_bindings/cuda/bindings/nvrtc.pxd b/cuda_bindings/cuda/bindings/nvrtc.pxd index 2e7ca2b505a..247992ac87d 100644 --- a/cuda_bindings/cuda/bindings/nvrtc.pxd +++ b/cuda_bindings/cuda/bindings/nvrtc.pxd @@ -2,7 +2,7 @@ # SPDX-License-Identifier: Apache-2.0 # This code was automatically generated with version 13.4.1. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=ba23f6c3908c2fa6496002f8def30ec166cec8643e4de22c1741040b2c4b2965 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=7b6ce83d58b42aae0455e262bb73a1c97c41e08e4ed6c8ec7dfb74e3cc754202 cimport cuda.bindings.cynvrtc as cynvrtc include "_lib/utils.pxd" @@ -57,5 +57,6 @@ cdef class nvrtcBundledHeadersInfo: getPtr() Get memory address of class instance """ + cdef object _owner cdef cynvrtc.nvrtcBundledHeadersInfo _pvt_val cdef cynvrtc.nvrtcBundledHeadersInfo* _pvt_ptr diff --git a/cuda_bindings/cuda/bindings/runtime.pxd b/cuda_bindings/cuda/bindings/runtime.pxd index 3665c0a1eba..e2c1125c753 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.4.1. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=7449c15b6137a39e8e9c26a3aee810954cead6b88b7c8a768abb9a2bc5875913 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=9aed2c4f6e06c8af7d8e05b8da369992de701809a2165dc6bd0cc05e135934f5 cimport cuda.bindings.cyruntime as cyruntime include "_lib/utils.pxd" @@ -320,6 +320,7 @@ cdef class dim3: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.dim3 _pvt_val cdef cyruntime.dim3* _pvt_ptr @@ -355,6 +356,7 @@ cdef class cudaChannelFormatDesc: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaChannelFormatDesc _pvt_val cdef cyruntime.cudaChannelFormatDesc* _pvt_ptr @@ -380,6 +382,7 @@ cdef class anon_struct0: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaArraySparseProperties* _pvt_ptr cdef class cudaArraySparseProperties: @@ -410,6 +413,7 @@ cdef class cudaArraySparseProperties: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaArraySparseProperties _pvt_val cdef cyruntime.cudaArraySparseProperties* _pvt_ptr @@ -436,6 +440,7 @@ cdef class cudaArrayMemoryRequirements: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaArrayMemoryRequirements _pvt_val cdef cyruntime.cudaArrayMemoryRequirements* _pvt_ptr @@ -467,6 +472,7 @@ cdef class cudaPitchedPtr: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaPitchedPtr _pvt_val cdef cyruntime.cudaPitchedPtr* _pvt_ptr @@ -498,6 +504,7 @@ cdef class cudaExtent: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExtent _pvt_val cdef cyruntime.cudaExtent* _pvt_ptr @@ -525,6 +532,7 @@ cdef class cudaPos: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaPos _pvt_val cdef cyruntime.cudaPos* _pvt_ptr @@ -572,6 +580,7 @@ cdef class cudaMemcpy3DParms: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemcpy3DParms _pvt_val cdef cyruntime.cudaMemcpy3DParms* _pvt_ptr @@ -621,6 +630,7 @@ cdef class cudaMemcpyNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemcpyNodeParams _pvt_val cdef cyruntime.cudaMemcpyNodeParams* _pvt_ptr @@ -678,6 +688,7 @@ cdef class cudaMemcpy3DPeerParms: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemcpy3DPeerParms _pvt_val cdef cyruntime.cudaMemcpy3DPeerParms* _pvt_ptr @@ -738,6 +749,7 @@ cdef class cudaMemsetParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemsetParams _pvt_val cdef cyruntime.cudaMemsetParams* _pvt_ptr @@ -785,6 +797,7 @@ cdef class cudaMemsetParamsV2: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemsetParamsV2 _pvt_val cdef cyruntime.cudaMemsetParamsV2* _pvt_ptr @@ -837,6 +850,7 @@ cdef class cudaAccessPolicyWindow: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaAccessPolicyWindow _pvt_val cdef cyruntime.cudaAccessPolicyWindow* _pvt_ptr @@ -863,6 +877,7 @@ cdef class cudaHostNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaHostNodeParams _pvt_val cdef cyruntime.cudaHostNodeParams* _pvt_ptr @@ -900,6 +915,7 @@ cdef class cudaHostNodeParamsV2: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaHostNodeParamsV2 _pvt_val cdef cyruntime.cudaHostNodeParamsV2* _pvt_ptr @@ -926,6 +942,7 @@ cdef class anon_struct1: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaResourceDesc* _pvt_ptr cdef cudaArray_t _array @@ -945,6 +962,7 @@ cdef class anon_struct2: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaResourceDesc* _pvt_ptr cdef cudaMipmappedArray_t _mipmap @@ -972,6 +990,7 @@ cdef class anon_struct3: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaResourceDesc* _pvt_ptr cdef _HelperInputVoidPtr _cydevPtr @@ -1010,6 +1029,7 @@ cdef class anon_struct4: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaResourceDesc* _pvt_ptr cdef _HelperInputVoidPtr _cydevPtr @@ -1025,6 +1045,7 @@ cdef class anon_struct5: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaResourceDesc* _pvt_ptr cdef class anon_union0: @@ -1053,6 +1074,7 @@ cdef class anon_union0: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaResourceDesc* _pvt_ptr cdef anon_struct1 _array @@ -1091,6 +1113,7 @@ cdef class cudaResourceDesc: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaResourceDesc* _val_ptr cdef cyruntime.cudaResourceDesc* _pvt_ptr @@ -1141,6 +1164,7 @@ cdef class cudaResourceViewDesc: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaResourceViewDesc _pvt_val cdef cyruntime.cudaResourceViewDesc* _pvt_ptr @@ -1187,6 +1211,7 @@ cdef class cudaPointerAttributes: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaPointerAttributes* _val_ptr cdef cyruntime.cudaPointerAttributes* _pvt_ptr @@ -1325,6 +1350,7 @@ cdef class cudaFuncAttributes: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaFuncAttributes _pvt_val cdef cyruntime.cudaFuncAttributes* _pvt_ptr @@ -1346,6 +1372,7 @@ cdef class anon_struct6: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemLocation* _pvt_ptr cdef class cudaMemLocation: @@ -1378,6 +1405,7 @@ cdef class cudaMemLocation: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemLocation* _val_ptr cdef cyruntime.cudaMemLocation* _pvt_ptr @@ -1404,6 +1432,7 @@ cdef class cudaMemAccessDesc: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemAccessDesc _pvt_val cdef cyruntime.cudaMemAccessDesc* _pvt_ptr @@ -1452,6 +1481,7 @@ cdef class cudaMemPoolProps: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemPoolProps _pvt_val cdef cyruntime.cudaMemPoolProps* _pvt_ptr @@ -1470,6 +1500,7 @@ cdef class cudaMemPoolPtrExportData: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemPoolPtrExportData _pvt_val cdef cyruntime.cudaMemPoolPtrExportData* _pvt_ptr @@ -1509,6 +1540,7 @@ cdef class cudaMemAllocNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemAllocNodeParams _pvt_val cdef cyruntime.cudaMemAllocNodeParams* _pvt_ptr @@ -1558,6 +1590,7 @@ cdef class cudaMemAllocNodeParamsV2: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemAllocNodeParamsV2 _pvt_val cdef cyruntime.cudaMemAllocNodeParamsV2* _pvt_ptr @@ -1587,6 +1620,7 @@ cdef class cudaMemFreeNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemFreeNodeParams _pvt_val cdef cyruntime.cudaMemFreeNodeParams* _pvt_ptr @@ -1626,6 +1660,7 @@ cdef class cudaMemcpyAttributes: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemcpyAttributes _pvt_val cdef cyruntime.cudaMemcpyAttributes* _pvt_ptr @@ -1659,6 +1694,7 @@ cdef class cudaOffset3D: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaOffset3D _pvt_val cdef cyruntime.cudaOffset3D* _pvt_ptr @@ -1688,6 +1724,7 @@ cdef class anon_struct7: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemcpy3DOperand* _pvt_ptr cdef _HelperInputVoidPtr _cyptr @@ -1714,6 +1751,7 @@ cdef class anon_struct8: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemcpy3DOperand* _pvt_ptr cdef cudaArray_t _array @@ -1740,6 +1778,7 @@ cdef class anon_union3: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemcpy3DOperand* _pvt_ptr cdef anon_struct7 _ptr @@ -1768,6 +1807,7 @@ cdef class cudaMemcpy3DOperand: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemcpy3DOperand* _val_ptr cdef cyruntime.cudaMemcpy3DOperand* _pvt_ptr @@ -1805,6 +1845,7 @@ cdef class cudaMemcpy3DBatchOp: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemcpy3DBatchOp _pvt_val cdef cyruntime.cudaMemcpy3DBatchOp* _pvt_ptr @@ -1831,6 +1872,7 @@ cdef class CUuuid_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.CUuuid_st _pvt_val cdef cyruntime.CUuuid_st* _pvt_ptr @@ -2237,6 +2279,7 @@ cdef class cudaDeviceProp: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaDeviceProp _pvt_val cdef cyruntime.cudaDeviceProp* _pvt_ptr @@ -2252,6 +2295,7 @@ cdef class cudaIpcEventHandle_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaIpcEventHandle_st _pvt_val cdef cyruntime.cudaIpcEventHandle_st* _pvt_ptr @@ -2264,6 +2308,7 @@ cdef class cudaIpcMemHandle_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaIpcMemHandle_st _pvt_val cdef cyruntime.cudaIpcMemHandle_st* _pvt_ptr @@ -2274,6 +2319,7 @@ cdef class cudaMemFabricHandle_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaMemFabricHandle_st _pvt_val cdef cyruntime.cudaMemFabricHandle_st* _pvt_ptr @@ -2295,6 +2341,7 @@ cdef class anon_struct9: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalMemoryHandleDesc* _pvt_ptr cdef _HelperInputVoidPtr _cyhandle @@ -2325,6 +2372,7 @@ cdef class anon_union4: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalMemoryHandleDesc* _pvt_ptr cdef anon_struct9 _win32 @@ -2361,6 +2409,7 @@ cdef class cudaExternalMemoryHandleDesc: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalMemoryHandleDesc* _val_ptr cdef cyruntime.cudaExternalMemoryHandleDesc* _pvt_ptr @@ -2391,6 +2440,7 @@ cdef class cudaExternalMemoryBufferDesc: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalMemoryBufferDesc _pvt_val cdef cyruntime.cudaExternalMemoryBufferDesc* _pvt_ptr @@ -2428,6 +2478,7 @@ cdef class cudaExternalMemoryMipmappedArrayDesc: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalMemoryMipmappedArrayDesc _pvt_val cdef cyruntime.cudaExternalMemoryMipmappedArrayDesc* _pvt_ptr @@ -2455,6 +2506,7 @@ cdef class anon_struct10: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreHandleDesc* _pvt_ptr cdef _HelperInputVoidPtr _cyhandle @@ -2485,6 +2537,7 @@ cdef class anon_union5: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreHandleDesc* _pvt_ptr cdef anon_struct10 _win32 @@ -2517,6 +2570,7 @@ cdef class cudaExternalSemaphoreHandleDesc: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreHandleDesc* _val_ptr cdef cyruntime.cudaExternalSemaphoreHandleDesc* _pvt_ptr @@ -2537,6 +2591,7 @@ cdef class anon_struct11: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreSignalParams* _pvt_ptr cdef class anon_union6: @@ -2553,6 +2608,7 @@ cdef class anon_union6: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreSignalParams* _pvt_ptr cdef _HelperInputVoidPtr _cyfence @@ -2572,6 +2628,7 @@ cdef class anon_struct12: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreSignalParams* _pvt_ptr cdef class anon_struct13: @@ -2596,6 +2653,7 @@ cdef class anon_struct13: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreSignalParams* _pvt_ptr cdef anon_struct11 _fence @@ -2634,6 +2692,7 @@ cdef class cudaExternalSemaphoreSignalParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreSignalParams _pvt_val cdef cyruntime.cudaExternalSemaphoreSignalParams* _pvt_ptr @@ -2654,6 +2713,7 @@ cdef class anon_struct14: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreWaitParams* _pvt_ptr cdef class anon_union7: @@ -2670,6 +2730,7 @@ cdef class anon_union7: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreWaitParams* _pvt_ptr cdef _HelperInputVoidPtr _cyfence @@ -2693,6 +2754,7 @@ cdef class anon_struct15: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreWaitParams* _pvt_ptr cdef class anon_struct16: @@ -2717,6 +2779,7 @@ cdef class anon_struct16: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreWaitParams* _pvt_ptr cdef anon_struct14 _fence @@ -2755,6 +2818,7 @@ cdef class cudaExternalSemaphoreWaitParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreWaitParams _pvt_val cdef cyruntime.cudaExternalSemaphoreWaitParams* _pvt_ptr @@ -2800,6 +2864,7 @@ cdef class cudaDevSmResource: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaDevSmResource _pvt_val cdef cyruntime.cudaDevSmResource* _pvt_ptr @@ -2827,6 +2892,7 @@ cdef class cudaDevWorkqueueConfigResource: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaDevWorkqueueConfigResource _pvt_val cdef cyruntime.cudaDevWorkqueueConfigResource* _pvt_ptr @@ -2839,6 +2905,7 @@ cdef class cudaDevWorkqueueResource: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaDevWorkqueueResource _pvt_val cdef cyruntime.cudaDevWorkqueueResource* _pvt_ptr @@ -2878,6 +2945,7 @@ cdef class cudaDevSmResourceGroupParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaDevSmResourceGroupParams_st _pvt_val cdef cyruntime.cudaDevSmResourceGroupParams_st* _pvt_ptr @@ -2936,6 +3004,7 @@ cdef class cudaDevResource_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaDevResource_st* _val_ptr cdef cyruntime.cudaDevResource_st* _pvt_ptr @@ -2978,6 +3047,7 @@ cdef class cudalibraryHostUniversalFunctionAndDataTable: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudalibraryHostUniversalFunctionAndDataTable _pvt_val cdef cyruntime.cudalibraryHostUniversalFunctionAndDataTable* _pvt_ptr @@ -3023,6 +3093,7 @@ cdef class cudaKernelNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaKernelNodeParams _pvt_val cdef cyruntime.cudaKernelNodeParams* _pvt_ptr @@ -3091,6 +3162,7 @@ cdef class cudaKernelNodeParamsV2: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaKernelNodeParamsV2* _val_ptr cdef cyruntime.cudaKernelNodeParamsV2* _pvt_ptr @@ -3140,6 +3212,7 @@ cdef class cudaExternalSemaphoreSignalNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreSignalNodeParams _pvt_val cdef cyruntime.cudaExternalSemaphoreSignalNodeParams* _pvt_ptr @@ -3180,6 +3253,7 @@ cdef class cudaExternalSemaphoreSignalNodeParamsV2: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreSignalNodeParamsV2 _pvt_val cdef cyruntime.cudaExternalSemaphoreSignalNodeParamsV2* _pvt_ptr @@ -3219,6 +3293,7 @@ cdef class cudaExternalSemaphoreWaitNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreWaitNodeParams _pvt_val cdef cyruntime.cudaExternalSemaphoreWaitNodeParams* _pvt_ptr @@ -3259,6 +3334,7 @@ cdef class cudaExternalSemaphoreWaitNodeParamsV2: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaExternalSemaphoreWaitNodeParamsV2 _pvt_val cdef cyruntime.cudaExternalSemaphoreWaitNodeParamsV2* _pvt_ptr @@ -3323,6 +3399,7 @@ cdef class cudaConditionalNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaConditionalNodeParams _pvt_val cdef cyruntime.cudaConditionalNodeParams* _pvt_ptr @@ -3360,6 +3437,7 @@ cdef class cudaChildGraphNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaChildGraphNodeParams _pvt_val cdef cyruntime.cudaChildGraphNodeParams* _pvt_ptr @@ -3386,6 +3464,7 @@ cdef class cudaEventRecordNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaEventRecordNodeParams _pvt_val cdef cyruntime.cudaEventRecordNodeParams* _pvt_ptr @@ -3411,6 +3490,7 @@ cdef class cudaEventWaitNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaEventWaitNodeParams _pvt_val cdef cyruntime.cudaEventWaitNodeParams* _pvt_ptr @@ -3481,6 +3561,7 @@ cdef class cudaGraphNodeParams: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaGraphNodeParams* _val_ptr cdef cyruntime.cudaGraphNodeParams* _pvt_ptr @@ -3562,6 +3643,7 @@ cdef class cudaGraphEdgeData_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaGraphEdgeData_st _pvt_val cdef cyruntime.cudaGraphEdgeData_st* _pvt_ptr @@ -3593,6 +3675,7 @@ cdef class cudaGraphInstantiateParams_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaGraphInstantiateParams_st _pvt_val cdef cyruntime.cudaGraphInstantiateParams_st* _pvt_ptr @@ -3629,6 +3712,7 @@ cdef class cudaGraphExecUpdateResultInfo_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaGraphExecUpdateResultInfo_st _pvt_val cdef cyruntime.cudaGraphExecUpdateResultInfo_st* _pvt_ptr @@ -3660,6 +3744,7 @@ cdef class anon_struct17: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaGraphKernelNodeUpdate* _pvt_ptr cdef _HelperInputVoidPtr _cypValue @@ -3687,6 +3772,7 @@ cdef class anon_union11: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaGraphKernelNodeUpdate* _pvt_ptr cdef dim3 _gridDim @@ -3721,6 +3807,7 @@ cdef class cudaGraphKernelNodeUpdate: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaGraphKernelNodeUpdate* _val_ptr cdef cyruntime.cudaGraphKernelNodeUpdate* _pvt_ptr @@ -3756,6 +3843,7 @@ cdef class cudaLaunchMemSyncDomainMap_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaLaunchMemSyncDomainMap_st _pvt_val cdef cyruntime.cudaLaunchMemSyncDomainMap_st* _pvt_ptr @@ -3781,6 +3869,7 @@ cdef class anon_struct18: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaLaunchAttributeValue* _pvt_ptr cdef class anon_struct19: @@ -3805,6 +3894,7 @@ cdef class anon_struct19: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaLaunchAttributeValue* _pvt_ptr cdef cudaEvent_t _event @@ -3832,6 +3922,7 @@ cdef class anon_struct20: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaLaunchAttributeValue* _pvt_ptr cdef class anon_struct21: @@ -3852,6 +3943,7 @@ cdef class anon_struct21: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaLaunchAttributeValue* _pvt_ptr cdef cudaEvent_t _event @@ -3875,6 +3967,7 @@ cdef class anon_struct22: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaLaunchAttributeValue* _pvt_ptr cdef cudaGraphDeviceNode_t _devNode @@ -4007,6 +4100,7 @@ cdef class cudaLaunchAttributeValue: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaLaunchAttributeValue _pvt_val cdef cyruntime.cudaLaunchAttributeValue* _pvt_ptr @@ -4051,6 +4145,7 @@ cdef class cudaLaunchAttribute_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaLaunchAttribute_st _pvt_val cdef cyruntime.cudaLaunchAttribute_st* _pvt_ptr @@ -4071,6 +4166,7 @@ cdef class anon_struct23: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaAsyncNotificationInfo* _pvt_ptr cdef class anon_union12: @@ -4087,6 +4183,7 @@ cdef class anon_union12: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaAsyncNotificationInfo* _pvt_ptr cdef anon_struct23 _overBudget @@ -4113,6 +4210,7 @@ cdef class cudaAsyncNotificationInfo: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaAsyncNotificationInfo* _val_ptr cdef cyruntime.cudaAsyncNotificationInfo* _pvt_ptr @@ -4183,6 +4281,7 @@ cdef class cudaTextureDesc: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaTextureDesc _pvt_val cdef cyruntime.cudaTextureDesc* _pvt_ptr @@ -4207,6 +4306,7 @@ cdef class cudaGraphRecaptureCallbackData: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaGraphRecaptureCallbackData _pvt_val cdef cyruntime.cudaGraphRecaptureCallbackData* _pvt_ptr @@ -4253,6 +4353,7 @@ cdef class cudaEglPlaneDesc_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaEglPlaneDesc_st _pvt_val cdef cyruntime.cudaEglPlaneDesc_st* _pvt_ptr @@ -4277,6 +4378,7 @@ cdef class anon_union13: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaEglFrame_st* _pvt_ptr cdef class cudaEglFrame_st: @@ -4318,6 +4420,7 @@ cdef class cudaEglFrame_st: getPtr() Get memory address of class instance """ + cdef object _owner cdef cyruntime.cudaEglFrame_st* _val_ptr cdef cyruntime.cudaEglFrame_st* _pvt_ptr diff --git a/cuda_bindings/cuda/bindings/runtime.pyx b/cuda_bindings/cuda/bindings/runtime.pyx index 087d6d4dfca..57771dcf933 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.4.1. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=685208d88a179bf2a468215105cfd8d90c9def1f1187bd1cef500ddbb69b50e7 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=21c0ed447e3e318a82a853cf7516c12214c48d0ceb0d9beb2be05157a8434ce1 from typing import Any, Optional import cython import ctypes @@ -8024,12 +8024,10 @@ cdef class cudaArraySparseProperties: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._tileExtent = anon_struct0(_ptr=self._pvt_ptr) - + self._tileExtent._owner = self def __dealloc__(self): - pass + self._tileExtent = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -8483,30 +8481,24 @@ cdef class cudaMemcpy3DParms: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._srcArray = cudaArray_t(_ptr=&self._pvt_ptr[0].srcArray) - - self._srcPos = cudaPos(_ptr=&self._pvt_ptr[0].srcPos) - - + self._srcPos._owner = self self._srcPtr = cudaPitchedPtr(_ptr=&self._pvt_ptr[0].srcPtr) - - + self._srcPtr._owner = self self._dstArray = cudaArray_t(_ptr=&self._pvt_ptr[0].dstArray) - - self._dstPos = cudaPos(_ptr=&self._pvt_ptr[0].dstPos) - - + self._dstPos._owner = self self._dstPtr = cudaPitchedPtr(_ptr=&self._pvt_ptr[0].dstPtr) - - + self._dstPtr._owner = self self._extent = cudaExtent(_ptr=&self._pvt_ptr[0].extent) - + self._extent._owner = self def __dealloc__(self): - pass + self._srcPos = None + self._srcPtr = None + self._dstPos = None + self._dstPtr = None + self._extent = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -8677,15 +8669,11 @@ cdef class cudaMemcpyNodeParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._ctx = cudaExecutionContext_t(_ptr=&self._pvt_ptr[0].ctx) - - self._copyParams = cudaMemcpy3DParms(_ptr=&self._pvt_ptr[0].copyParams) - + self._copyParams._owner = self def __dealloc__(self): - pass + self._copyParams = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -8800,30 +8788,24 @@ cdef class cudaMemcpy3DPeerParms: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._srcArray = cudaArray_t(_ptr=&self._pvt_ptr[0].srcArray) - - self._srcPos = cudaPos(_ptr=&self._pvt_ptr[0].srcPos) - - + self._srcPos._owner = self self._srcPtr = cudaPitchedPtr(_ptr=&self._pvt_ptr[0].srcPtr) - - + self._srcPtr._owner = self self._dstArray = cudaArray_t(_ptr=&self._pvt_ptr[0].dstArray) - - self._dstPos = cudaPos(_ptr=&self._pvt_ptr[0].dstPos) - - + self._dstPos._owner = self self._dstPtr = cudaPitchedPtr(_ptr=&self._pvt_ptr[0].dstPtr) - - + self._dstPtr._owner = self self._extent = cudaExtent(_ptr=&self._pvt_ptr[0].extent) - + self._extent._owner = self def __dealloc__(self): - pass + self._srcPos = None + self._srcPtr = None + self._dstPos = None + self._dstPtr = None + self._extent = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -9163,10 +9145,7 @@ cdef class cudaMemsetParamsV2: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._ctx = cudaExecutionContext_t(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): pass def getPtr(self): @@ -9444,10 +9423,7 @@ cdef class cudaHostNodeParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._fn = cudaHostFn_t(_ptr=&self._pvt_ptr[0].fn) - def __dealloc__(self): pass def getPtr(self): @@ -9531,13 +9507,8 @@ cdef class cudaHostNodeParamsV2: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._fn = cudaHostFn_t(_ptr=&self._pvt_ptr[0].fn) - - self._ctx = cudaExecutionContext_t(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): pass def getPtr(self): @@ -9642,10 +9613,7 @@ cdef class anon_struct1: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._array = cudaArray_t(_ptr=&self._pvt_ptr[0].res.array.array) - def __dealloc__(self): pass def getPtr(self): @@ -9698,10 +9666,7 @@ cdef class anon_struct2: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._mipmap = cudaMipmappedArray_t(_ptr=&self._pvt_ptr[0].res.mipmap.mipmap) - def __dealloc__(self): pass def getPtr(self): @@ -9762,12 +9727,10 @@ cdef class anon_struct3: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._desc = cudaChannelFormatDesc(_ptr=&self._pvt_ptr[0].res.linear.desc) - + self._desc._owner = self def __dealloc__(self): - pass + self._desc = None def getPtr(self): return &self._pvt_ptr[0].res.linear def __repr__(self): @@ -9854,12 +9817,10 @@ cdef class anon_struct4: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._desc = cudaChannelFormatDesc(_ptr=&self._pvt_ptr[0].res.pitch2D.desc) - + self._desc._owner = self def __dealloc__(self): - pass + self._desc = None def getPtr(self): return &self._pvt_ptr[0].res.pitch2D def __repr__(self): @@ -9994,21 +9955,19 @@ cdef class anon_union0: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._array = anon_struct1(_ptr=self._pvt_ptr) - - + self._array._owner = self self._mipmap = anon_struct2(_ptr=self._pvt_ptr) - - + self._mipmap._owner = self self._linear = anon_struct3(_ptr=self._pvt_ptr) - - + self._linear._owner = self self._pitch2D = anon_struct4(_ptr=self._pvt_ptr) - + self._pitch2D._owner = self def __dealloc__(self): - pass + self._array = None + self._mipmap = None + self._linear = None + self._pitch2D = None def getPtr(self): return &self._pvt_ptr[0].res def __repr__(self): @@ -10105,11 +10064,10 @@ cdef class cudaResourceDesc: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._res = anon_union0(_ptr=self._pvt_ptr) - + self._res._owner = self def __dealloc__(self): + self._res = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -10970,11 +10928,10 @@ cdef class cudaMemLocation: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._localized = anon_struct6(_ptr=self._pvt_ptr) - + self._localized._owner = self def __dealloc__(self): + self._localized = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -11054,12 +11011,10 @@ cdef class cudaMemAccessDesc: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._location = cudaMemLocation(_ptr=&self._pvt_ptr[0].location) - + self._location._owner = self def __dealloc__(self): - pass + self._location = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -11145,12 +11100,10 @@ cdef class cudaMemPoolProps: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._location = cudaMemLocation(_ptr=&self._pvt_ptr[0].location) - + self._location._owner = self def __dealloc__(self): - pass + self._location = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -11315,16 +11268,13 @@ cdef class cudaMemAllocNodeParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._poolProps = cudaMemPoolProps(_ptr=&self._pvt_ptr[0].poolProps) - + self._poolProps._owner = self def __dealloc__(self): - + self._poolProps = None if self._accessDescs is not NULL: free(self._accessDescs) self._pvt_ptr[0].accessDescs = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -11374,8 +11324,12 @@ cdef class cudaMemAllocNodeParams: @property def accessDescs(self): - arrs = [self._pvt_ptr[0].accessDescs + x*sizeof(cyruntime.cudaMemAccessDesc) for x in range(self._accessDescs_length)] - return [cudaMemAccessDesc(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].accessDescs == NULL: + return [] + out_accessDescs = [cudaMemAccessDesc() for _idx in range(self._accessDescs_length)] + for _idx in range(len(out_accessDescs)): + string.memcpy(out_accessDescs[_idx].getPtr(), &self._pvt_ptr[0].accessDescs[_idx], sizeof(cyruntime.cudaMemAccessDesc)) + return out_accessDescs @accessDescs.setter def accessDescs(self, val): cdef cyruntime.cudaMemAccessDesc* _accessDescs_new @@ -11386,10 +11340,6 @@ cdef class cudaMemAllocNodeParams: self._pvt_ptr[0].accessDescs = NULL else: if self._accessDescs_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _accessDescs_new = calloc(len(val), sizeof(cyruntime.cudaMemAccessDesc)) if _accessDescs_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cyruntime.cudaMemAccessDesc))) @@ -11404,7 +11354,6 @@ cdef class cudaMemAllocNodeParams: string.memcpy(&self._accessDescs[idx], (val[idx])._pvt_ptr, sizeof(cyruntime.cudaMemAccessDesc)) - @property def accessDescCount(self): return self._pvt_ptr[0].accessDescCount @@ -11472,16 +11421,13 @@ cdef class cudaMemAllocNodeParamsV2: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._poolProps = cudaMemPoolProps(_ptr=&self._pvt_ptr[0].poolProps) - + self._poolProps._owner = self def __dealloc__(self): - + self._poolProps = None if self._accessDescs is not NULL: free(self._accessDescs) self._pvt_ptr[0].accessDescs = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -11531,8 +11477,12 @@ cdef class cudaMemAllocNodeParamsV2: @property def accessDescs(self): - arrs = [self._pvt_ptr[0].accessDescs + x*sizeof(cyruntime.cudaMemAccessDesc) for x in range(self._accessDescs_length)] - return [cudaMemAccessDesc(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].accessDescs == NULL: + return [] + out_accessDescs = [cudaMemAccessDesc() for _idx in range(self._accessDescs_length)] + for _idx in range(len(out_accessDescs)): + string.memcpy(out_accessDescs[_idx].getPtr(), &self._pvt_ptr[0].accessDescs[_idx], sizeof(cyruntime.cudaMemAccessDesc)) + return out_accessDescs @accessDescs.setter def accessDescs(self, val): cdef cyruntime.cudaMemAccessDesc* _accessDescs_new @@ -11543,10 +11493,6 @@ cdef class cudaMemAllocNodeParamsV2: self._pvt_ptr[0].accessDescs = NULL else: if self._accessDescs_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _accessDescs_new = calloc(len(val), sizeof(cyruntime.cudaMemAccessDesc)) if _accessDescs_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cyruntime.cudaMemAccessDesc))) @@ -11561,7 +11507,6 @@ cdef class cudaMemAllocNodeParamsV2: string.memcpy(&self._accessDescs[idx], (val[idx])._pvt_ptr, sizeof(cyruntime.cudaMemAccessDesc)) - @property def accessDescCount(self): return self._pvt_ptr[0].accessDescCount @@ -11675,15 +11620,13 @@ cdef class cudaMemcpyAttributes: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._srcLocHint = cudaMemLocation(_ptr=&self._pvt_ptr[0].srcLocHint) - - + self._srcLocHint._owner = self self._dstLocHint = cudaMemLocation(_ptr=&self._pvt_ptr[0].dstLocHint) - + self._dstLocHint._owner = self def __dealloc__(self): - pass + self._srcLocHint = None + self._dstLocHint = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -11863,12 +11806,10 @@ cdef class anon_struct7: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._locHint = cudaMemLocation(_ptr=&self._pvt_ptr[0].op.ptr.locHint) - + self._locHint._owner = self def __dealloc__(self): - pass + self._locHint = None def getPtr(self): return &self._pvt_ptr[0].op.ptr def __repr__(self): @@ -11957,15 +11898,11 @@ cdef class anon_struct8: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._array = cudaArray_t(_ptr=&self._pvt_ptr[0].op.array.array) - - self._offset = cudaOffset3D(_ptr=&self._pvt_ptr[0].op.array.offset) - + self._offset._owner = self def __dealloc__(self): - pass + self._offset = None def getPtr(self): return &self._pvt_ptr[0].op.array def __repr__(self): @@ -12034,15 +11971,13 @@ cdef class anon_union3: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._ptr = anon_struct7(_ptr=self._pvt_ptr) - - + self._ptr._owner = self self._array = anon_struct8(_ptr=self._pvt_ptr) - + self._array._owner = self def __dealloc__(self): - pass + self._ptr = None + self._array = None def getPtr(self): return &self._pvt_ptr[0].op def __repr__(self): @@ -12107,11 +12042,10 @@ cdef class cudaMemcpy3DOperand: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._op = anon_union3(_ptr=self._pvt_ptr) - + self._op._owner = self def __dealloc__(self): + self._op = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -12188,18 +12122,16 @@ cdef class cudaMemcpy3DBatchOp: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._src = cudaMemcpy3DOperand(_ptr=&self._pvt_ptr[0].src) - - + self._src._owner = self self._dst = cudaMemcpy3DOperand(_ptr=&self._pvt_ptr[0].dst) - - + self._dst._owner = self self._extent = cudaExtent(_ptr=&self._pvt_ptr[0].extent) - + self._extent._owner = self def __dealloc__(self): - pass + self._src = None + self._dst = None + self._extent = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -12731,12 +12663,10 @@ cdef class cudaDeviceProp: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._uuid = cudaUUID_t(_ptr=&self._pvt_ptr[0].uuid) - + self._uuid._owner = self def __dealloc__(self): - pass + self._uuid = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -14218,12 +14148,10 @@ cdef class anon_union4: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._win32 = anon_struct9(_ptr=self._pvt_ptr) - + self._win32._owner = self def __dealloc__(self): - pass + self._win32 = None def getPtr(self): return &self._pvt_ptr[0].handle def __repr__(self): @@ -14311,11 +14239,10 @@ cdef class cudaExternalMemoryHandleDesc: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._handle = anon_union4(_ptr=self._pvt_ptr) - + self._handle._owner = self def __dealloc__(self): + self._handle = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -14507,15 +14434,13 @@ cdef class cudaExternalMemoryMipmappedArrayDesc: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._formatDesc = cudaChannelFormatDesc(_ptr=&self._pvt_ptr[0].formatDesc) - - + self._formatDesc._owner = self self._extent = cudaExtent(_ptr=&self._pvt_ptr[0].extent) - + self._extent._owner = self def __dealloc__(self): - pass + self._formatDesc = None + self._extent = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -14685,12 +14610,10 @@ cdef class anon_union5: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._win32 = anon_struct10(_ptr=self._pvt_ptr) - + self._win32._owner = self def __dealloc__(self): - pass + self._win32 = None def getPtr(self): return &self._pvt_ptr[0].handle def __repr__(self): @@ -14774,11 +14697,10 @@ cdef class cudaExternalSemaphoreHandleDesc: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._handle = anon_union5(_ptr=self._pvt_ptr) - + self._handle._owner = self def __dealloc__(self): + self._handle = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -14991,18 +14913,16 @@ cdef class anon_struct13: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._fence = anon_struct11(_ptr=self._pvt_ptr) - - + self._fence._owner = self self._nvSciSync = anon_union6(_ptr=self._pvt_ptr) - - + self._nvSciSync._owner = self self._keyedMutex = anon_struct12(_ptr=self._pvt_ptr) - + self._keyedMutex._owner = self def __dealloc__(self): - pass + self._fence = None + self._nvSciSync = None + self._keyedMutex = None def getPtr(self): return &self._pvt_ptr[0].params def __repr__(self): @@ -15087,12 +15007,10 @@ cdef class cudaExternalSemaphoreSignalParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._params = anon_struct13(_ptr=self._pvt_ptr) - + self._params._owner = self def __dealloc__(self): - pass + self._params = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -15307,18 +15225,16 @@ cdef class anon_struct16: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._fence = anon_struct14(_ptr=self._pvt_ptr) - - + self._fence._owner = self self._nvSciSync = anon_union7(_ptr=self._pvt_ptr) - - + self._nvSciSync._owner = self self._keyedMutex = anon_struct15(_ptr=self._pvt_ptr) - + self._keyedMutex._owner = self def __dealloc__(self): - pass + self._fence = None + self._nvSciSync = None + self._keyedMutex = None def getPtr(self): return &self._pvt_ptr[0].params def __repr__(self): @@ -15403,12 +15319,10 @@ cdef class cudaExternalSemaphoreWaitParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._params = anon_struct16(_ptr=self._pvt_ptr) - + self._params._owner = self def __dealloc__(self): - pass + self._params = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -15871,22 +15785,19 @@ cdef class cudaDevResource_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._sm = cudaDevSmResource(_ptr=&self._pvt_ptr[0].sm) - - + self._sm._owner = self self._wqConfig = cudaDevWorkqueueConfigResource(_ptr=&self._pvt_ptr[0].wqConfig) - - + self._wqConfig._owner = self self._wq = cudaDevWorkqueueResource(_ptr=&self._pvt_ptr[0].wq) - + self._wq._owner = self def __dealloc__(self): - + self._sm = None + self._wqConfig = None + self._wq = None if self._nextResource is not NULL: free(self._nextResource) self._pvt_ptr[0].nextResource = NULL - if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -15996,8 +15907,12 @@ cdef class cudaDevResource_st: @property def nextResource(self): - arrs = [self._pvt_ptr[0].nextResource + x*sizeof(cyruntime.cudaDevResource_st) for x in range(self._nextResource_length)] - return [cudaDevResource_st(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].nextResource == NULL: + return [] + out_nextResource = [cudaDevResource_st() for _idx in range(self._nextResource_length)] + for _idx in range(len(out_nextResource)): + string.memcpy(out_nextResource[_idx].getPtr(), &self._pvt_ptr[0].nextResource[_idx], sizeof(cyruntime.cudaDevResource_st)) + return out_nextResource @nextResource.setter def nextResource(self, val): cdef cyruntime.cudaDevResource_st* _nextResource_new @@ -16008,10 +15923,6 @@ cdef class cudaDevResource_st: self._pvt_ptr[0].nextResource = NULL else: if self._nextResource_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _nextResource_new = calloc(len(val), sizeof(cyruntime.cudaDevResource_st)) if _nextResource_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cyruntime.cudaDevResource_st))) @@ -16026,7 +15937,6 @@ cdef class cudaDevResource_st: string.memcpy(&self._nextResource[idx], (val[idx])._pvt_ptr, sizeof(cyruntime.cudaDevResource_st)) - cdef class cudalibraryHostUniversalFunctionAndDataTable: """ Attributes @@ -16171,15 +16081,13 @@ cdef class cudaKernelNodeParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._gridDim = dim3(_ptr=&self._pvt_ptr[0].gridDim) - - + self._gridDim._owner = self self._blockDim = dim3(_ptr=&self._pvt_ptr[0].blockDim) - + self._blockDim._owner = self def __dealloc__(self): - pass + self._gridDim = None + self._blockDim = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -16264,7 +16172,7 @@ cdef class cudaKernelNodeParams: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams @property @@ -16335,23 +16243,16 @@ cdef class cudaKernelNodeParamsV2: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._kern = cudaKernel_t(_ptr=&self._pvt_ptr[0].kern) - - self._cuFunc = cudaFunction_t(_ptr=&self._pvt_ptr[0].cuFunc) - - self._gridDim = dim3(_ptr=&self._pvt_ptr[0].gridDim) - - + self._gridDim._owner = self self._blockDim = dim3(_ptr=&self._pvt_ptr[0].blockDim) - - + self._blockDim._owner = self self._ctx = cudaExecutionContext_t(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): + self._gridDim = None + self._blockDim = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -16496,7 +16397,7 @@ cdef class cudaKernelNodeParamsV2: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams @property @@ -16565,16 +16466,12 @@ cdef class cudaExternalSemaphoreSignalNodeParams: def __init__(self, void_ptr _ptr = 0): pass def __dealloc__(self): - if self._extSemArray is not NULL: free(self._extSemArray) self._pvt_ptr[0].extSemArray = NULL - - if self._paramsArray is not NULL: free(self._paramsArray) self._pvt_ptr[0].paramsArray = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -16628,8 +16525,12 @@ cdef class cudaExternalSemaphoreSignalNodeParams: @property def paramsArray(self): - arrs = [self._pvt_ptr[0].paramsArray + x*sizeof(cyruntime.cudaExternalSemaphoreSignalParams) for x in range(self._paramsArray_length)] - return [cudaExternalSemaphoreSignalParams(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].paramsArray == NULL: + return [] + out_paramsArray = [cudaExternalSemaphoreSignalParams() for _idx in range(self._paramsArray_length)] + for _idx in range(len(out_paramsArray)): + string.memcpy(out_paramsArray[_idx].getPtr(), &self._pvt_ptr[0].paramsArray[_idx], sizeof(cyruntime.cudaExternalSemaphoreSignalParams)) + return out_paramsArray @paramsArray.setter def paramsArray(self, val): cdef cyruntime.cudaExternalSemaphoreSignalParams* _paramsArray_new @@ -16640,10 +16541,6 @@ cdef class cudaExternalSemaphoreSignalNodeParams: self._pvt_ptr[0].paramsArray = NULL else: if self._paramsArray_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _paramsArray_new = calloc(len(val), sizeof(cyruntime.cudaExternalSemaphoreSignalParams)) if _paramsArray_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cyruntime.cudaExternalSemaphoreSignalParams))) @@ -16658,7 +16555,6 @@ cdef class cudaExternalSemaphoreSignalNodeParams: string.memcpy(&self._paramsArray[idx], (val[idx])._pvt_ptr, sizeof(cyruntime.cudaExternalSemaphoreSignalParams)) - @property def numExtSems(self): return self._pvt_ptr[0].numExtSems @@ -16702,21 +16598,14 @@ cdef class cudaExternalSemaphoreSignalNodeParamsV2: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._ctx = cudaExecutionContext_t(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): - if self._extSemArray is not NULL: free(self._extSemArray) self._pvt_ptr[0].extSemArray = NULL - - if self._paramsArray is not NULL: free(self._paramsArray) self._pvt_ptr[0].paramsArray = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -16776,8 +16665,12 @@ cdef class cudaExternalSemaphoreSignalNodeParamsV2: @property def paramsArray(self): - arrs = [self._pvt_ptr[0].paramsArray + x*sizeof(cyruntime.cudaExternalSemaphoreSignalParams) for x in range(self._paramsArray_length)] - return [cudaExternalSemaphoreSignalParams(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].paramsArray == NULL: + return [] + out_paramsArray = [cudaExternalSemaphoreSignalParams() for _idx in range(self._paramsArray_length)] + for _idx in range(len(out_paramsArray)): + string.memcpy(out_paramsArray[_idx].getPtr(), &self._pvt_ptr[0].paramsArray[_idx], sizeof(cyruntime.cudaExternalSemaphoreSignalParams)) + return out_paramsArray @paramsArray.setter def paramsArray(self, val): cdef cyruntime.cudaExternalSemaphoreSignalParams* _paramsArray_new @@ -16788,10 +16681,6 @@ cdef class cudaExternalSemaphoreSignalNodeParamsV2: self._pvt_ptr[0].paramsArray = NULL else: if self._paramsArray_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _paramsArray_new = calloc(len(val), sizeof(cyruntime.cudaExternalSemaphoreSignalParams)) if _paramsArray_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cyruntime.cudaExternalSemaphoreSignalParams))) @@ -16806,7 +16695,6 @@ cdef class cudaExternalSemaphoreSignalNodeParamsV2: string.memcpy(&self._paramsArray[idx], (val[idx])._pvt_ptr, sizeof(cyruntime.cudaExternalSemaphoreSignalParams)) - @property def numExtSems(self): return self._pvt_ptr[0].numExtSems @@ -16865,16 +16753,12 @@ cdef class cudaExternalSemaphoreWaitNodeParams: def __init__(self, void_ptr _ptr = 0): pass def __dealloc__(self): - if self._extSemArray is not NULL: free(self._extSemArray) self._pvt_ptr[0].extSemArray = NULL - - if self._paramsArray is not NULL: free(self._paramsArray) self._pvt_ptr[0].paramsArray = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -16928,8 +16812,12 @@ cdef class cudaExternalSemaphoreWaitNodeParams: @property def paramsArray(self): - arrs = [self._pvt_ptr[0].paramsArray + x*sizeof(cyruntime.cudaExternalSemaphoreWaitParams) for x in range(self._paramsArray_length)] - return [cudaExternalSemaphoreWaitParams(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].paramsArray == NULL: + return [] + out_paramsArray = [cudaExternalSemaphoreWaitParams() for _idx in range(self._paramsArray_length)] + for _idx in range(len(out_paramsArray)): + string.memcpy(out_paramsArray[_idx].getPtr(), &self._pvt_ptr[0].paramsArray[_idx], sizeof(cyruntime.cudaExternalSemaphoreWaitParams)) + return out_paramsArray @paramsArray.setter def paramsArray(self, val): cdef cyruntime.cudaExternalSemaphoreWaitParams* _paramsArray_new @@ -16940,10 +16828,6 @@ cdef class cudaExternalSemaphoreWaitNodeParams: self._pvt_ptr[0].paramsArray = NULL else: if self._paramsArray_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _paramsArray_new = calloc(len(val), sizeof(cyruntime.cudaExternalSemaphoreWaitParams)) if _paramsArray_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cyruntime.cudaExternalSemaphoreWaitParams))) @@ -16958,7 +16842,6 @@ cdef class cudaExternalSemaphoreWaitNodeParams: string.memcpy(&self._paramsArray[idx], (val[idx])._pvt_ptr, sizeof(cyruntime.cudaExternalSemaphoreWaitParams)) - @property def numExtSems(self): return self._pvt_ptr[0].numExtSems @@ -17002,21 +16885,14 @@ cdef class cudaExternalSemaphoreWaitNodeParamsV2: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._ctx = cudaExecutionContext_t(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): - if self._extSemArray is not NULL: free(self._extSemArray) self._pvt_ptr[0].extSemArray = NULL - - if self._paramsArray is not NULL: free(self._paramsArray) self._pvt_ptr[0].paramsArray = NULL - def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -17076,8 +16952,12 @@ cdef class cudaExternalSemaphoreWaitNodeParamsV2: @property def paramsArray(self): - arrs = [self._pvt_ptr[0].paramsArray + x*sizeof(cyruntime.cudaExternalSemaphoreWaitParams) for x in range(self._paramsArray_length)] - return [cudaExternalSemaphoreWaitParams(_ptr=arr) for arr in arrs] + if self._pvt_ptr[0].paramsArray == NULL: + return [] + out_paramsArray = [cudaExternalSemaphoreWaitParams() for _idx in range(self._paramsArray_length)] + for _idx in range(len(out_paramsArray)): + string.memcpy(out_paramsArray[_idx].getPtr(), &self._pvt_ptr[0].paramsArray[_idx], sizeof(cyruntime.cudaExternalSemaphoreWaitParams)) + return out_paramsArray @paramsArray.setter def paramsArray(self, val): cdef cyruntime.cudaExternalSemaphoreWaitParams* _paramsArray_new @@ -17088,10 +16968,6 @@ cdef class cudaExternalSemaphoreWaitNodeParamsV2: self._pvt_ptr[0].paramsArray = NULL else: if self._paramsArray_length != len(val): - # Allocate and fill a new buffer before touching the - # live state so a failure leaves this object unchanged - # (strong exception guarantee); the old buffer is only - # freed once the resize is known to succeed. _paramsArray_new = calloc(len(val), sizeof(cyruntime.cudaExternalSemaphoreWaitParams)) if _paramsArray_new is NULL: raise MemoryError('Failed to allocate length x size memory: ' + str(len(val)) + 'x' + str(sizeof(cyruntime.cudaExternalSemaphoreWaitParams))) @@ -17106,7 +16982,6 @@ cdef class cudaExternalSemaphoreWaitNodeParamsV2: string.memcpy(&self._paramsArray[idx], (val[idx])._pvt_ptr, sizeof(cyruntime.cudaExternalSemaphoreWaitParams)) - @property def numExtSems(self): return self._pvt_ptr[0].numExtSems @@ -17188,13 +17063,8 @@ cdef class cudaConditionalNodeParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._handle = cudaGraphConditionalHandle(_ptr=&self._pvt_ptr[0].handle) - - self._ctx = cudaExecutionContext_t(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): pass def getPtr(self): @@ -17323,10 +17193,7 @@ cdef class cudaChildGraphNodeParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._graph = cudaGraph_t(_ptr=&self._pvt_ptr[0].graph) - def __dealloc__(self): pass def getPtr(self): @@ -17401,13 +17268,8 @@ cdef class cudaEventRecordNodeParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._event = cudaEvent_t(_ptr=&self._pvt_ptr[0].event) - - self._ctx = cudaExecutionContext_t(_ptr=&self._pvt_ptr[0].ctx) - def __dealloc__(self): pass def getPtr(self): @@ -17487,10 +17349,7 @@ cdef class cudaEventWaitNodeParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._event = cudaEvent_t(_ptr=&self._pvt_ptr[0].event) - def __dealloc__(self): pass def getPtr(self): @@ -17596,44 +17455,43 @@ cdef class cudaGraphNodeParams: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._kernel = cudaKernelNodeParamsV2(_ptr=&self._pvt_ptr[0].kernel) - - + self._kernel._owner = self self._memcpy = cudaMemcpyNodeParams(_ptr=&self._pvt_ptr[0].memcpy) - - + self._memcpy._owner = self self._memset = cudaMemsetParamsV2(_ptr=&self._pvt_ptr[0].memset) - - + self._memset._owner = self self._host = cudaHostNodeParamsV2(_ptr=&self._pvt_ptr[0].host) - - + self._host._owner = self self._graph = cudaChildGraphNodeParams(_ptr=&self._pvt_ptr[0].graph) - - + self._graph._owner = self self._eventWait = cudaEventWaitNodeParams(_ptr=&self._pvt_ptr[0].eventWait) - - + self._eventWait._owner = self self._eventRecord = cudaEventRecordNodeParams(_ptr=&self._pvt_ptr[0].eventRecord) - - + self._eventRecord._owner = self self._extSemSignal = cudaExternalSemaphoreSignalNodeParamsV2(_ptr=&self._pvt_ptr[0].extSemSignal) - - + self._extSemSignal._owner = self self._extSemWait = cudaExternalSemaphoreWaitNodeParamsV2(_ptr=&self._pvt_ptr[0].extSemWait) - - + self._extSemWait._owner = self self._alloc = cudaMemAllocNodeParamsV2(_ptr=&self._pvt_ptr[0].alloc) - - + self._alloc._owner = self self._free = cudaMemFreeNodeParams(_ptr=&self._pvt_ptr[0].free) - - + self._free._owner = self self._conditional = cudaConditionalNodeParams(_ptr=&self._pvt_ptr[0].conditional) - + self._conditional._owner = self def __dealloc__(self): + self._kernel = None + self._memcpy = None + self._memset = None + self._host = None + self._graph = None + self._eventWait = None + self._eventRecord = None + self._extSemSignal = None + self._extSemWait = None + self._alloc = None + self._free = None + self._conditional = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -17963,13 +17821,8 @@ cdef class cudaGraphInstantiateParams_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._uploadStream = cudaStream_t(_ptr=&self._pvt_ptr[0].uploadStream) - - self._errNode_out = cudaGraphNode_t(_ptr=&self._pvt_ptr[0].errNode_out) - def __dealloc__(self): pass def getPtr(self): @@ -18088,13 +17941,8 @@ cdef class cudaGraphExecUpdateResultInfo_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._errorNode = cudaGraphNode_t(_ptr=&self._pvt_ptr[0].errorNode) - - self._errorFromNode = cudaGraphNode_t(_ptr=&self._pvt_ptr[0].errorFromNode) - def __dealloc__(self): pass def getPtr(self): @@ -18273,15 +18121,13 @@ cdef class anon_union11: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._gridDim = dim3(_ptr=&self._pvt_ptr[0].updateData.gridDim) - - + self._gridDim._owner = self self._param = anon_struct17(_ptr=self._pvt_ptr) - + self._param._owner = self def __dealloc__(self): - pass + self._gridDim = None + self._param = None def getPtr(self): return &self._pvt_ptr[0].updateData def __repr__(self): @@ -18366,14 +18212,11 @@ cdef class cudaGraphKernelNodeUpdate: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._node = cudaGraphDeviceNode_t(_ptr=&self._pvt_ptr[0].node) - - self._updateData = anon_union11(_ptr=self._pvt_ptr) - + self._updateData._owner = self def __dealloc__(self): + self._updateData = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -18614,10 +18457,7 @@ cdef class anon_struct19: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._event = cudaEvent_t(_ptr=&self._pvt_ptr[0].programmaticEvent.event) - def __dealloc__(self): pass def getPtr(self): @@ -18782,10 +18622,7 @@ cdef class anon_struct21: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._event = cudaEvent_t(_ptr=&self._pvt_ptr[0].launchCompletionEvent.event) - def __dealloc__(self): pass def getPtr(self): @@ -18856,10 +18693,7 @@ cdef class anon_struct22: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._devNode = cudaGraphDeviceNode_t(_ptr=&self._pvt_ptr[0].deviceUpdatableKernelNode.devNode) - def __dealloc__(self): pass def getPtr(self): @@ -19041,30 +18875,28 @@ cdef class cudaLaunchAttributeValue: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._accessPolicyWindow = cudaAccessPolicyWindow(_ptr=&self._pvt_ptr[0].accessPolicyWindow) - - + self._accessPolicyWindow._owner = self self._clusterDim = anon_struct18(_ptr=self._pvt_ptr) - - + self._clusterDim._owner = self self._programmaticEvent = anon_struct19(_ptr=self._pvt_ptr) - - + self._programmaticEvent._owner = self self._memSyncDomainMap = cudaLaunchMemSyncDomainMap(_ptr=&self._pvt_ptr[0].memSyncDomainMap) - - + self._memSyncDomainMap._owner = self self._preferredClusterDim = anon_struct20(_ptr=self._pvt_ptr) - - + self._preferredClusterDim._owner = self self._launchCompletionEvent = anon_struct21(_ptr=self._pvt_ptr) - - + self._launchCompletionEvent._owner = self self._deviceUpdatableKernelNode = anon_struct22(_ptr=self._pvt_ptr) - + self._deviceUpdatableKernelNode._owner = self def __dealloc__(self): - pass + self._accessPolicyWindow = None + self._clusterDim = None + self._programmaticEvent = None + self._memSyncDomainMap = None + self._preferredClusterDim = None + self._launchCompletionEvent = None + self._deviceUpdatableKernelNode = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -19363,12 +19195,10 @@ cdef class cudaLaunchAttribute_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._val = cudaLaunchAttributeValue(_ptr=&self._pvt_ptr[0].val) - + self._val._owner = self def __dealloc__(self): - pass + self._val = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -19468,12 +19298,10 @@ cdef class anon_union12: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr): - pass - self._overBudget = anon_struct23(_ptr=self._pvt_ptr) - + self._overBudget._owner = self def __dealloc__(self): - pass + self._overBudget = None def getPtr(self): return &self._pvt_ptr[0].info def __repr__(self): @@ -19525,11 +19353,10 @@ cdef class cudaAsyncNotificationInfo: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._info = anon_union12(_ptr=self._pvt_ptr) - + self._info._owner = self def __dealloc__(self): + self._info = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): @@ -19860,10 +19687,7 @@ cdef class cudaGraphRecaptureCallbackData: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._callbackFunc = cudaGraphRecaptureCallback_t(_ptr=&self._pvt_ptr[0].callbackFunc) - def __dealloc__(self): pass def getPtr(self): @@ -19956,12 +19780,10 @@ cdef class cudaEglPlaneDesc_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._channelDesc = cudaChannelFormatDesc(_ptr=&self._pvt_ptr[0].channelDesc) - + self._channelDesc._owner = self def __dealloc__(self): - pass + self._channelDesc = None def getPtr(self): return self._pvt_ptr def __repr__(self): @@ -20175,11 +19997,10 @@ cdef class cudaEglFrame_st: else: self._pvt_ptr = _ptr def __init__(self, void_ptr _ptr = 0): - pass - self._frame = anon_union13(_ptr=self._pvt_ptr) - + self._frame._owner = self def __dealloc__(self): + self._frame = None if self._val_ptr is not NULL: free(self._val_ptr) def getPtr(self): From 20f1320d32312958204a595d242a907ea24f989a Mon Sep 17 00:00:00 2001 From: "Ralf W. Grosse-Kunstleve" Date: Fri, 25 Sep 2026 21:58:25 -0700 Subject: [PATCH 2/5] run_cybind_native 13.4.2 ../post_mr574_public_refresh (NO MANUAL CHANGES) --- cuda_bindings/cuda/bindings/nvml.pyx | 24 ++++++++---------------- 1 file changed, 8 insertions(+), 16 deletions(-) diff --git a/cuda_bindings/cuda/bindings/nvml.pyx b/cuda_bindings/cuda/bindings/nvml.pyx index a713a667e07..1f264e666c0 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.4.1. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=11827bb18f0653afd95163d1d140a0ec529d3d025b1ca1da61f96ee88f48d948 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=149bd04cef4a762c554f5f82eaf15ab823a608acea1fca906b5981dfa96baa8a # <<<< PREAMBLE CONTENT >>>> @@ -24523,7 +24523,7 @@ cdef class NvlinkFirmwareInfo: """NvlinkFirmwareVersion: OUT - NVLINK firmware version.""" return NvlinkFirmwareVersion.from_ptr( &(self._ptr[0].firmwareVersion), - 100, + self._ptr[0].numValidEntries, readonly=self._readonly, owner=self, ) @@ -24533,20 +24533,12 @@ cdef class NvlinkFirmwareInfo: if self._readonly: raise ValueError("This NvlinkFirmwareInfo instance is read-only") cdef NvlinkFirmwareVersion val_ = val - if len(val) != 100: - raise ValueError(f"Expected length { 100 } for field firmware_version, got {len(val)}") - _cyb_memcpy(&(self._ptr[0].firmwareVersion), (val_._get_ptr()), sizeof(nvmlNvlinkFirmwareVersion_t) * 100) - - @property - def num_valid_entries(self): - """int: OUT - Number of valid firmware entries.""" - return self._ptr[0].numValidEntries - - @num_valid_entries.setter - def num_valid_entries(self, val): - if self._readonly: - raise ValueError("This NvlinkFirmwareInfo instance is read-only") - self._ptr[0].numValidEntries = val + if len(val) > 100: + raise ValueError(f"Expected length < 100 for field firmware_version, got {len(val)}") + self._ptr[0].numValidEntries = len(val) + if len(val) == 0: + return + _cyb_memcpy(&(self._ptr[0].firmwareVersion), (val_._get_ptr()), sizeof(nvmlNvlinkFirmwareVersion_t) * self._ptr[0].numValidEntries) @staticmethod def from_buffer(buffer): From 6f04788ab0d25e705d82e56beb6e4f8c6e14a099 Mon Sep 17 00:00:00 2001 From: "Ralf W. Grosse-Kunstleve" Date: Sat, 26 Sep 2026 14:12:05 -0700 Subject: [PATCH 3/5] Regenerate CUDA 13.4 bindings with direct kernel parameter access --- cuda_bindings/cuda/bindings/driver.pyx | 16 ++++++++-------- cuda_bindings/cuda/bindings/runtime.pyx | 6 +++--- 2 files changed, 11 insertions(+), 11 deletions(-) diff --git a/cuda_bindings/cuda/bindings/driver.pyx b/cuda_bindings/cuda/bindings/driver.pyx index c999fb467f4..a6570e88b39 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.4.1. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=09b7034a85e8350f14d2f4170ff1d2ecfd97fc292bfd920ee428dafc0e9ecf1e +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=175f5b5d51fbe64e7d8f5eca92e8b557cab5dea406091f66e10a4d19400dcefa from typing import Any, Optional import cython import ctypes @@ -11826,7 +11826,7 @@ cdef class CUDA_KERNEL_NODE_PARAMS_st: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams @property @@ -12070,7 +12070,7 @@ cdef class CUDA_KERNEL_NODE_PARAMS_v2_st: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams @property @@ -12348,7 +12348,7 @@ cdef class CUDA_KERNEL_NODE_PARAMS_v3_st: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams @property @@ -18425,7 +18425,7 @@ cdef class CUDA_LAUNCH_PARAMS_st: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams cdef class anon_struct12: @@ -43462,7 +43462,7 @@ def cuLaunchKernel(f, unsigned int gridDimX, unsigned int gridDimY, unsigned int pf = int(CUfunction(f)) cyf = pf cdef _HelperKernelParams cykernelParams = _HelperKernelParams(kernelParams) - cdef void** cykernelParams_ptr = cykernelParams.ckernelParams + cdef void** cykernelParams_ptr = cykernelParams.ckernelParams with nogil: err = cydriver.cuLaunchKernel(cyf, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, cyhStream, cykernelParams_ptr, extra) return (_CUresult(err),) @@ -43700,7 +43700,7 @@ def cuLaunchKernelEx(config : Optional[CUlaunchConfig], f, kernelParams, void_pt cyf = pf cdef cydriver.CUlaunchConfig* cyconfig_ptr = config._pvt_ptr if config is not None else NULL cdef _HelperKernelParams cykernelParams = _HelperKernelParams(kernelParams) - cdef void** cykernelParams_ptr = cykernelParams.ckernelParams + cdef void** cykernelParams_ptr = cykernelParams.ckernelParams with nogil: err = cydriver.cuLaunchKernelEx(cyconfig_ptr, cyf, cykernelParams_ptr, extra) return (_CUresult(err),) @@ -43810,7 +43810,7 @@ def cuLaunchCooperativeKernel(f, unsigned int gridDimX, unsigned int gridDimY, u pf = int(CUfunction(f)) cyf = pf cdef _HelperKernelParams cykernelParams = _HelperKernelParams(kernelParams) - cdef void** cykernelParams_ptr = cykernelParams.ckernelParams + cdef void** cykernelParams_ptr = cykernelParams.ckernelParams with nogil: err = cydriver.cuLaunchCooperativeKernel(cyf, gridDimX, gridDimY, gridDimZ, blockDimX, blockDimY, blockDimZ, sharedMemBytes, cyhStream, cykernelParams_ptr) return (_CUresult(err),) diff --git a/cuda_bindings/cuda/bindings/runtime.pyx b/cuda_bindings/cuda/bindings/runtime.pyx index 57771dcf933..2b61ac54135 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.4.1. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=21c0ed447e3e318a82a853cf7516c12214c48d0ceb0d9beb2be05157a8434ce1 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=4c952a0aa0dcb7a2948769d3eee64d0ef217ca1a8bd72873d99d94e9a34f2a65 from typing import Any, Optional import cython import ctypes @@ -16172,7 +16172,7 @@ cdef class cudaKernelNodeParams: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams @property @@ -16397,7 +16397,7 @@ cdef class cudaKernelNodeParamsV2: @kernelParams.setter def kernelParams(self, kernelParams): self._cykernelParams = _HelperKernelParams(kernelParams) - self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams + self._pvt_ptr[0].kernelParams = self._cykernelParams.ckernelParams @property From 4fb9840c6fa18da48fe9aca25007e61511c2cdab Mon Sep 17 00:00:00 2001 From: "Ralf W. Grosse-Kunstleve" Date: Sun, 27 Sep 2026 11:01:38 -0700 Subject: [PATCH 4/5] run_cybind_cython_gen 13.4.2 ../post_mr574_public_refresh (NO MANUAL CHANGES) after adding commit 797a08ab9d2262fb11ba7d7207e1a66495f818fc to cybind !580 --- cuda_bindings/cuda/bindings/cyruntime.pxd | 5 +---- 1 file changed, 1 insertion(+), 4 deletions(-) diff --git a/cuda_bindings/cuda/bindings/cyruntime.pxd b/cuda_bindings/cuda/bindings/cyruntime.pxd index 3bd31653dd3..2d705a6be16 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.4.1. Do not modify it directly. -# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=f18e04577ef4372076f7baaf4adeeb91967e3c809bfdd0e4b1224d0d9ded81e2 +# CYTHON-BINDINGS-GENERATED-DO-NOT-MODIFY-THIS-FILE: format=1; content-sha256=c3643e519b69bdb09b9c4c6ff3ecd3aebb180636d00e9a7bd2fe129cbed3eeb4 from libc.stdint cimport uint32_t, uint64_t @@ -2674,9 +2674,6 @@ cdef extern from 'cuda_runtime_api.h': cdef enum: CUDA_EGL_MAX_PLANES = 3 -# cudaDevSmResourceGroupLocalityDomainIdAny is defined as (~0u) in driver_types.h; the -# pyclibrary-based cython-gen parser can't evaluate that expression, so hardcode the value - # libraryPropertyType_t (starts lowercase, outside type pattern) cdef extern from 'library_types.h': ctypedef enum libraryPropertyType_t 'libraryPropertyType_t': From d2eabbf774621d698d8ec6b561ba12708929c0b5 Mon Sep 17 00:00:00 2001 From: Michael Droettboom Date: Wed, 30 Sep 2026 15:01:44 -0400 Subject: [PATCH 5/5] Add release note about NvJitlinkFirmwareInfo --- cuda_bindings/docs/source/release/13.5.0-notes.rst | 4 ++++ 1 file changed, 4 insertions(+) diff --git a/cuda_bindings/docs/source/release/13.5.0-notes.rst b/cuda_bindings/docs/source/release/13.5.0-notes.rst index cb1f16e8fe4..24beb455284 100644 --- a/cuda_bindings/docs/source/release/13.5.0-notes.rst +++ b/cuda_bindings/docs/source/release/13.5.0-notes.rst @@ -284,6 +284,10 @@ Changes (and the redundant ``sample_count`` — which was only ever the array's own size — is no longer part of the returned value; use ``len(result)`` instead). +- ``nvml.NvlinkFirmwareInfo``: The ``firmware_version`` member now returns only + valid entries. The ``num_valid_entries`` member is removed, as its design made + it possible to access invalid memory. + Enhancements ------------