diff --git a/lib/cublas/libcublas.jl b/lib/cublas/libcublas.jl index 6642bf4068..7cd1d3d9e6 100644 --- a/lib/cublas/libcublas.jl +++ b/lib/cublas/libcublas.jl @@ -3048,6 +3048,7 @@ end CUBLAS_PEDANTIC_MATH = 2 CUBLAS_TF32_TENSOR_OP_MATH = 3 CUBLAS_FP32_EMULATED_BF16X9_MATH = 4 + CUBLAS_FP64_EMULATED_FIXEDPOINT_MATH = 8 CUBLAS_MATH_DISALLOW_REDUCED_PRECISION_REDUCTION = 16 end @@ -3064,6 +3065,7 @@ const cublasDataType_t = cudaDataType CUBLAS_COMPUTE_32F_EMULATED_16BFX9 = 78 CUBLAS_COMPUTE_64F = 70 CUBLAS_COMPUTE_64F_PEDANTIC = 71 + CUBLAS_COMPUTE_64F_EMULATED_FIXEDPOINT = 79 CUBLAS_COMPUTE_32I = 72 CUBLAS_COMPUTE_32I_PEDANTIC = 73 end @@ -3134,6 +3136,70 @@ end emulationStrategy::cublasEmulationStrategy_t)::cublasStatus_t end +@checked function cublasGetEmulationSpecialValuesSupport(handle, mask) + initialize_context() + @gcsafe_ccall libcublas.cublasGetEmulationSpecialValuesSupport(handle::cublasHandle_t, + mask::Ptr{cudaEmulationSpecialValuesSupport})::cublasStatus_t +end + +@checked function cublasSetEmulationSpecialValuesSupport(handle, mask) + initialize_context() + @gcsafe_ccall libcublas.cublasSetEmulationSpecialValuesSupport(handle::cublasHandle_t, + mask::cudaEmulationSpecialValuesSupport)::cublasStatus_t +end + +@checked function cublasGetFixedPointEmulationMantissaControl(handle, mantissaControl) + initialize_context() + @gcsafe_ccall libcublas.cublasGetFixedPointEmulationMantissaControl(handle::cublasHandle_t, + mantissaControl::Ptr{cudaEmulationMantissaControl})::cublasStatus_t +end + +@checked function cublasSetFixedPointEmulationMantissaControl(handle, mantissaControl) + initialize_context() + @gcsafe_ccall libcublas.cublasSetFixedPointEmulationMantissaControl(handle::cublasHandle_t, + mantissaControl::cudaEmulationMantissaControl)::cublasStatus_t +end + +@checked function cublasGetFixedPointEmulationMaxMantissaBitCount(handle, + maxMantissaBitCount) + initialize_context() + @gcsafe_ccall libcublas.cublasGetFixedPointEmulationMaxMantissaBitCount(handle::cublasHandle_t, + maxMantissaBitCount::Ptr{Cint})::cublasStatus_t +end + +@checked function cublasSetFixedPointEmulationMaxMantissaBitCount(handle, + maxMantissaBitCount) + initialize_context() + @gcsafe_ccall libcublas.cublasSetFixedPointEmulationMaxMantissaBitCount(handle::cublasHandle_t, + maxMantissaBitCount::Cint)::cublasStatus_t +end + +@checked function cublasGetFixedPointEmulationMantissaBitOffset(handle, mantissaBitOffset) + initialize_context() + @gcsafe_ccall libcublas.cublasGetFixedPointEmulationMantissaBitOffset(handle::cublasHandle_t, + mantissaBitOffset::Ptr{Cint})::cublasStatus_t +end + +@checked function cublasSetFixedPointEmulationMantissaBitOffset(handle, mantissaBitOffset) + initialize_context() + @gcsafe_ccall libcublas.cublasSetFixedPointEmulationMantissaBitOffset(handle::cublasHandle_t, + mantissaBitOffset::Cint)::cublasStatus_t +end + +@checked function cublasGetFixedPointEmulationMantissaBitCountPointer(handle, + mantissaBitCount) + initialize_context() + @gcsafe_ccall libcublas.cublasGetFixedPointEmulationMantissaBitCountPointer(handle::cublasHandle_t, + mantissaBitCount::Ptr{Ptr{Cint}})::cublasStatus_t +end + +@checked function cublasSetFixedPointEmulationMantissaBitCountPointer(handle, + mantissaBitCount) + initialize_context() + @gcsafe_ccall libcublas.cublasSetFixedPointEmulationMantissaBitCountPointer(handle::cublasHandle_t, + mantissaBitCount::Ptr{Cint})::cublasStatus_t +end + function cublasGetStatusName(status) initialize_context() @gcsafe_ccall libcublas.cublasGetStatusName(status::cublasStatus_t)::Cstring diff --git a/lib/cublas/libcublasLt.jl b/lib/cublas/libcublasLt.jl index 7b93b965d5..9abacf1e3a 100644 --- a/lib/cublas/libcublasLt.jl +++ b/lib/cublas/libcublasLt.jl @@ -86,6 +86,12 @@ end const cublasLtMatmulPreference_t = Ptr{cublasLtMatmulPreferenceOpaque_t} +struct cublasLtEmulationDescOpaque_t + data::NTuple{8,UInt64} +end + +const cublasLtEmulationDesc_t = Ptr{cublasLtEmulationDescOpaque_t} + @cenum cublasLtMatmulTile_t::UInt32 begin CUBLASLT_MATMUL_TILE_UNDEFINED = 0 CUBLASLT_MATMUL_TILE_8x8 = 1 @@ -998,6 +1004,7 @@ end CUBLASLT_MATMUL_DESC_EPILOGUE_AUX_SCALE_MODE = 35 CUBLASLT_MATMUL_DESC_D_OUT_SCALE_POINTER = 36 CUBLASLT_MATMUL_DESC_D_OUT_SCALE_MODE = 37 + CUBLASLT_MATMUL_DESC_EMULATION_DESCRIPTOR = 38 end @checked function cublasLtMatmulDescInit_internal(matmulDesc, size, computeType, scaleType) @@ -1095,6 +1102,54 @@ end sizeWritten::Ptr{Csize_t})::cublasStatus_t end +@cenum cublasLtEmulationDescAttributes_t::UInt32 begin + CUBLASLT_EMULATION_DESC_STRATEGY = 0 + CUBLASLT_EMULATION_DESC_SPECIAL_VALUES_SUPPORT = 1 + CUBLASLT_EMULATION_DESC_FIXEDPOINT_MANTISSA_CONTROL = 2 + CUBLASLT_EMULATION_DESC_FIXEDPOINT_MAX_MANTISSA_BIT_COUNT = 3 + CUBLASLT_EMULATION_DESC_FIXEDPOINT_MANTISSA_BIT_OFFSET = 4 + CUBLASLT_EMULATION_DESC_FIXEDPOINT_MANTISSA_BIT_COUNT_POINTER = 5 +end + +@checked function cublasLtEmulationDescInit_internal(emulationDesc, size) + initialize_context() + @gcsafe_ccall libcublasLt.cublasLtEmulationDescInit_internal(emulationDesc::cublasLtEmulationDesc_t, + size::Csize_t)::cublasStatus_t +end + +@checked function cublasLtEmulationDescInit(emulationDesc) + initialize_context() + @gcsafe_ccall libcublasLt.cublasLtEmulationDescInit(emulationDesc::cublasLtEmulationDesc_t)::cublasStatus_t +end + +@checked function cublasLtEmulationDescCreate(emulationDesc) + initialize_context() + @gcsafe_ccall libcublasLt.cublasLtEmulationDescCreate(emulationDesc::Ptr{cublasLtEmulationDesc_t})::cublasStatus_t +end + +@checked function cublasLtEmulationDescDestroy(emulationDesc) + initialize_context() + @gcsafe_ccall libcublasLt.cublasLtEmulationDescDestroy(emulationDesc::cublasLtEmulationDesc_t)::cublasStatus_t +end + +@checked function cublasLtEmulationDescSetAttribute(emulationDesc, attr, buf, sizeInBytes) + initialize_context() + @gcsafe_ccall libcublasLt.cublasLtEmulationDescSetAttribute(emulationDesc::cublasLtEmulationDesc_t, + attr::cublasLtEmulationDescAttributes_t, + buf::Ptr{Cvoid}, + sizeInBytes::Csize_t)::cublasStatus_t +end + +@checked function cublasLtEmulationDescGetAttribute(emulationDesc, attr, buf, sizeInBytes, + sizeWritten) + initialize_context() + @gcsafe_ccall libcublasLt.cublasLtEmulationDescGetAttribute(emulationDesc::cublasLtEmulationDesc_t, + attr::cublasLtEmulationDescAttributes_t, + buf::Ptr{Cvoid}, + sizeInBytes::Csize_t, + sizeWritten::Ptr{Csize_t})::cublasStatus_t +end + @cenum cublasLtReductionScheme_t::UInt32 begin CUBLASLT_REDUCTION_SCHEME_NONE = 0 CUBLASLT_REDUCTION_SCHEME_INPLACE = 1 @@ -1344,7 +1399,7 @@ end @gcsafe_ccall libcublasLt.cublasLtLoggerSetMask(mask::Cint)::cublasStatus_t end -# no prototype is found for this function at cublasLt.h:2521:29, please use with caution +# no prototype is found for this function at cublasLt.h:2670:29, please use with caution @checked function cublasLtLoggerForceDisable() initialize_context() @gcsafe_ccall libcublasLt.cublasLtLoggerForceDisable()::cublasStatus_t diff --git a/lib/cudadrv/libcuda.jl b/lib/cudadrv/libcuda.jl index 0bce3afd40..0eba6a017c 100644 --- a/lib/cudadrv/libcuda.jl +++ b/lib/cudadrv/libcuda.jl @@ -165,27 +165,27 @@ end const CUexecAffinityType = CUexecAffinityType_enum -struct var"##Ctag#253" +struct var"##Ctag#298" data::NTuple{4,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#253"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#298"}, f::Symbol) f === :smCount && return Ptr{CUexecAffinitySmCount}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#253", f::Symbol) - r = Ref{var"##Ctag#253"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#253"}, r) +function Base.getproperty(x::var"##Ctag#298", f::Symbol) + r = Ref{var"##Ctag#298"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#298"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#253"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#298"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#253", private::Bool=false) +function Base.propertynames(x::var"##Ctag#298", private::Bool=false) return (:smCount, if private fieldnames(typeof(x)) else @@ -199,7 +199,7 @@ end function Base.getproperty(x::Ptr{CUexecAffinityParam_st}, f::Symbol) f === :type && return Ptr{CUexecAffinityType}(x + 0) - f === :param && return Ptr{var"##Ctag#253"}(x + 4) + f === :param && return Ptr{var"##Ctag#298"}(x + 4) return getfield(x, f) end @@ -571,28 +571,28 @@ end const CUmemcpy3DOperandType = CUmemcpy3DOperandType_enum -struct var"##Ctag#265" +struct var"##Ctag#310" data::NTuple{32,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#265"}, f::Symbol) - f === :ptr && return Ptr{var"##Ctag#266"}(x + 0) - f === :array && return Ptr{var"##Ctag#267"}(x + 0) +function Base.getproperty(x::Ptr{var"##Ctag#310"}, f::Symbol) + f === :ptr && return Ptr{var"##Ctag#311"}(x + 0) + f === :array && return Ptr{var"##Ctag#312"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#265", f::Symbol) - r = Ref{var"##Ctag#265"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#265"}, r) +function Base.getproperty(x::var"##Ctag#310", f::Symbol) + r = Ref{var"##Ctag#310"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#310"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#265"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#310"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#265", private::Bool=false) +function Base.propertynames(x::var"##Ctag#310", private::Bool=false) return (:ptr, :array, if private fieldnames(typeof(x)) else @@ -606,7 +606,7 @@ end function Base.getproperty(x::Ptr{CUmemcpy3DOperand_st}, f::Symbol) f === :type && return Ptr{CUmemcpy3DOperandType}(x + 0) - f === :op && return Ptr{var"##Ctag#265"}(x + 8) + f === :op && return Ptr{var"##Ctag#310"}(x + 8) return getfield(x, f) end @@ -1602,27 +1602,27 @@ end const CUasyncNotificationType = CUasyncNotificationType_enum -struct var"##Ctag#239" +struct var"##Ctag#284" data::NTuple{8,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#239"}, f::Symbol) - f === :overBudget && return Ptr{var"##Ctag#240"}(x + 0) +function Base.getproperty(x::Ptr{var"##Ctag#284"}, f::Symbol) + f === :overBudget && return Ptr{var"##Ctag#285"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#239", f::Symbol) - r = Ref{var"##Ctag#239"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#239"}, r) +function Base.getproperty(x::var"##Ctag#284", f::Symbol) + r = Ref{var"##Ctag#284"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#284"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#239"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#284"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#239", private::Bool=false) +function Base.propertynames(x::var"##Ctag#284", private::Bool=false) return (:overBudget, if private fieldnames(typeof(x)) else @@ -1636,7 +1636,7 @@ end function Base.getproperty(x::Ptr{CUasyncNotificationInfo_st}, f::Symbol) f === :type && return Ptr{CUasyncNotificationType}(x + 0) - f === :info && return Ptr{var"##Ctag#239"}(x + 8) + f === :info && return Ptr{var"##Ctag#284"}(x + 8) return getfield(x, f) end @@ -2258,16 +2258,16 @@ function Base.getproperty(x::Ptr{CUlaunchAttributeValue_union}, f::Symbol) f === :accessPolicyWindow && return Ptr{CUaccessPolicyWindow}(x + 0) f === :cooperative && return Ptr{Cint}(x + 0) f === :syncPolicy && return Ptr{CUsynchronizationPolicy}(x + 0) - f === :clusterDim && return Ptr{var"##Ctag#247"}(x + 0) + f === :clusterDim && return Ptr{var"##Ctag#292"}(x + 0) f === :clusterSchedulingPolicyPreference && return Ptr{CUclusterSchedulingPolicy}(x + 0) f === :programmaticStreamSerializationAllowed && return Ptr{Cint}(x + 0) - f === :programmaticEvent && return Ptr{var"##Ctag#248"}(x + 0) - f === :launchCompletionEvent && return Ptr{var"##Ctag#249"}(x + 0) + f === :programmaticEvent && return Ptr{var"##Ctag#293"}(x + 0) + f === :launchCompletionEvent && return Ptr{var"##Ctag#294"}(x + 0) f === :priority && return Ptr{Cint}(x + 0) f === :memSyncDomainMap && return Ptr{CUlaunchMemSyncDomainMap}(x + 0) f === :memSyncDomain && return Ptr{CUlaunchMemSyncDomain}(x + 0) - f === :preferredClusterDim && return Ptr{var"##Ctag#250"}(x + 0) - f === :deviceUpdatableKernelNode && return Ptr{var"##Ctag#251"}(x + 0) + f === :preferredClusterDim && return Ptr{var"##Ctag#295"}(x + 0) + f === :deviceUpdatableKernelNode && return Ptr{var"##Ctag#296"}(x + 0) f === :sharedMemCarveout && return Ptr{Cuint}(x + 0) f === :nvlinkUtilCentricScheduling && return Ptr{Cuint}(x + 0) return getfield(x, f) @@ -2479,26 +2479,26 @@ end const CUDA_MEMCPY_NODE_PARAMS = CUDA_MEMCPY_NODE_PARAMS_st -struct var"##Ctag#264" +struct var"##Ctag#309" width::Cuint height::Cuint depth::Cuint end -function Base.getproperty(x::Ptr{var"##Ctag#264"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#309"}, f::Symbol) f === :width && return Ptr{Cuint}(x + 0) f === :height && return Ptr{Cuint}(x + 4) f === :depth && return Ptr{Cuint}(x + 8) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#264", f::Symbol) - r = Ref{var"##Ctag#264"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#264"}, r) +function Base.getproperty(x::var"##Ctag#309", f::Symbol) + r = Ref{var"##Ctag#309"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#309"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#264"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#309"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end @@ -2507,7 +2507,7 @@ struct CUDA_ARRAY_SPARSE_PROPERTIES_st end function Base.getproperty(x::Ptr{CUDA_ARRAY_SPARSE_PROPERTIES_st}, f::Symbol) - f === :tileExtent && return Ptr{var"##Ctag#264"}(x + 0) + f === :tileExtent && return Ptr{var"##Ctag#309"}(x + 0) f === :miptailFirstLevel && return Ptr{Cuint}(x + 12) f === :miptailSize && return Ptr{Culonglong}(x + 16) f === :flags && return Ptr{Cuint}(x + 24) @@ -2549,31 +2549,31 @@ const CUDA_ARRAY_MEMORY_REQUIREMENTS_v1 = CUDA_ARRAY_MEMORY_REQUIREMENTS_st const CUDA_ARRAY_MEMORY_REQUIREMENTS = CUDA_ARRAY_MEMORY_REQUIREMENTS_v1 -struct var"##Ctag#258" +struct var"##Ctag#303" data::NTuple{128,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#258"}, f::Symbol) - f === :array && return Ptr{var"##Ctag#259"}(x + 0) - f === :mipmap && return Ptr{var"##Ctag#260"}(x + 0) - f === :linear && return Ptr{var"##Ctag#261"}(x + 0) - f === :pitch2D && return Ptr{var"##Ctag#262"}(x + 0) - f === :reserved && return Ptr{var"##Ctag#263"}(x + 0) +function Base.getproperty(x::Ptr{var"##Ctag#303"}, f::Symbol) + f === :array && return Ptr{var"##Ctag#304"}(x + 0) + f === :mipmap && return Ptr{var"##Ctag#305"}(x + 0) + f === :linear && return Ptr{var"##Ctag#306"}(x + 0) + f === :pitch2D && return Ptr{var"##Ctag#307"}(x + 0) + f === :reserved && return Ptr{var"##Ctag#308"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#258", f::Symbol) - r = Ref{var"##Ctag#258"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#258"}, r) +function Base.getproperty(x::var"##Ctag#303", f::Symbol) + r = Ref{var"##Ctag#303"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#303"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#258"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#303"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#258", private::Bool=false) +function Base.propertynames(x::var"##Ctag#303", private::Bool=false) return (:array, :mipmap, :linear, :pitch2D, :reserved, if private fieldnames(typeof(x)) else @@ -2587,7 +2587,7 @@ end function Base.getproperty(x::Ptr{CUDA_RESOURCE_DESC_st}, f::Symbol) f === :resType && return Ptr{CUresourcetype}(x + 0) - f === :res && return Ptr{var"##Ctag#258"}(x + 8) + f === :res && return Ptr{var"##Ctag#303"}(x + 8) f === :flags && return Ptr{Cuint}(x + 136) return getfield(x, f) end @@ -2830,29 +2830,29 @@ end const CUexternalMemoryHandleType = CUexternalMemoryHandleType_enum -struct var"##Ctag#241" +struct var"##Ctag#286" data::NTuple{16,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#241"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#286"}, f::Symbol) f === :fd && return Ptr{Cint}(x + 0) - f === :win32 && return Ptr{var"##Ctag#242"}(x + 0) + f === :win32 && return Ptr{var"##Ctag#287"}(x + 0) f === :nvSciBufObject && return Ptr{Ptr{Cvoid}}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#241", f::Symbol) - r = Ref{var"##Ctag#241"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#241"}, r) +function Base.getproperty(x::var"##Ctag#286", f::Symbol) + r = Ref{var"##Ctag#286"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#286"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#241"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#286"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#241", private::Bool=false) +function Base.propertynames(x::var"##Ctag#286", private::Bool=false) return (:fd, :win32, :nvSciBufObject, if private fieldnames(typeof(x)) else @@ -2866,7 +2866,7 @@ end function Base.getproperty(x::Ptr{CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st}, f::Symbol) f === :type && return Ptr{CUexternalMemoryHandleType}(x + 0) - f === :handle && return Ptr{var"##Ctag#241"}(x + 8) + f === :handle && return Ptr{var"##Ctag#286"}(x + 8) f === :size && return Ptr{Culonglong}(x + 24) f === :flags && return Ptr{Cuint}(x + 32) f === :reserved && return Ptr{NTuple{16,Cuint}}(x + 36) @@ -2933,29 +2933,29 @@ end const CUexternalSemaphoreHandleType = CUexternalSemaphoreHandleType_enum -struct var"##Ctag#232" +struct var"##Ctag#277" data::NTuple{16,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#232"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#277"}, f::Symbol) f === :fd && return Ptr{Cint}(x + 0) - f === :win32 && return Ptr{var"##Ctag#233"}(x + 0) + f === :win32 && return Ptr{var"##Ctag#278"}(x + 0) f === :nvSciSyncObj && return Ptr{Ptr{Cvoid}}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#232", f::Symbol) - r = Ref{var"##Ctag#232"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#232"}, r) +function Base.getproperty(x::var"##Ctag#277", f::Symbol) + r = Ref{var"##Ctag#277"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#277"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#232"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#277"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#232", private::Bool=false) +function Base.propertynames(x::var"##Ctag#277", private::Bool=false) return (:fd, :win32, :nvSciSyncObj, if private fieldnames(typeof(x)) else @@ -2969,7 +2969,7 @@ end function Base.getproperty(x::Ptr{CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st}, f::Symbol) f === :type && return Ptr{CUexternalSemaphoreHandleType}(x + 0) - f === :handle && return Ptr{var"##Ctag#232"}(x + 8) + f === :handle && return Ptr{var"##Ctag#277"}(x + 8) f === :flags && return Ptr{Cuint}(x + 24) f === :reserved && return Ptr{NTuple{16,Cuint}}(x + 28) return getfield(x, f) @@ -2998,47 +2998,47 @@ const CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_v1 = CUDA_EXTERNAL_SEMAPHORE_HANDLE_DE const CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC = CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_v1 -struct var"##Ctag#255" +struct var"##Ctag#300" value::Culonglong end -function Base.getproperty(x::Ptr{var"##Ctag#255"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#300"}, f::Symbol) f === :value && return Ptr{Culonglong}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#255", f::Symbol) - r = Ref{var"##Ctag#255"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#255"}, r) +function Base.getproperty(x::var"##Ctag#300", f::Symbol) + r = Ref{var"##Ctag#300"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#300"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#255"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#300"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#256" +struct var"##Ctag#301" data::NTuple{8,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#256"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#301"}, f::Symbol) f === :fence && return Ptr{Ptr{Cvoid}}(x + 0) f === :reserved && return Ptr{Culonglong}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#256", f::Symbol) - r = Ref{var"##Ctag#256"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#256"}, r) +function Base.getproperty(x::var"##Ctag#301", f::Symbol) + r = Ref{var"##Ctag#301"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#301"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#256"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#301"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#256", private::Bool=false) +function Base.propertynames(x::var"##Ctag#301", private::Bool=false) return (:fence, :reserved, if private fieldnames(typeof(x)) else @@ -3046,49 +3046,49 @@ function Base.propertynames(x::var"##Ctag#256", private::Bool=false) end...) end -struct var"##Ctag#257" +struct var"##Ctag#302" key::Culonglong end -function Base.getproperty(x::Ptr{var"##Ctag#257"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#302"}, f::Symbol) f === :key && return Ptr{Culonglong}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#257", f::Symbol) - r = Ref{var"##Ctag#257"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#257"}, r) +function Base.getproperty(x::var"##Ctag#302", f::Symbol) + r = Ref{var"##Ctag#302"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#302"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#257"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#302"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#254" +struct var"##Ctag#299" data::NTuple{72,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#254"}, f::Symbol) - f === :fence && return Ptr{var"##Ctag#255"}(x + 0) - f === :nvSciSync && return Ptr{var"##Ctag#256"}(x + 8) - f === :keyedMutex && return Ptr{var"##Ctag#257"}(x + 16) +function Base.getproperty(x::Ptr{var"##Ctag#299"}, f::Symbol) + f === :fence && return Ptr{var"##Ctag#300"}(x + 0) + f === :nvSciSync && return Ptr{var"##Ctag#301"}(x + 8) + f === :keyedMutex && return Ptr{var"##Ctag#302"}(x + 16) f === :reserved && return Ptr{NTuple{12,Cuint}}(x + 24) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#254", f::Symbol) - r = Ref{var"##Ctag#254"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#254"}, r) +function Base.getproperty(x::var"##Ctag#299", f::Symbol) + r = Ref{var"##Ctag#299"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#299"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#254"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#299"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#254", private::Bool=false) +function Base.propertynames(x::var"##Ctag#299", private::Bool=false) return (:fence, :nvSciSync, :keyedMutex, :reserved, if private fieldnames(typeof(x)) else @@ -3131,47 +3131,47 @@ const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_v1 = CUDA_EXTERNAL_SEMAPHORE_SIGNAL_ const CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS = CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_v1 -struct var"##Ctag#244" +struct var"##Ctag#289" value::Culonglong end -function Base.getproperty(x::Ptr{var"##Ctag#244"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#289"}, f::Symbol) f === :value && return Ptr{Culonglong}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#244", f::Symbol) - r = Ref{var"##Ctag#244"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#244"}, r) +function Base.getproperty(x::var"##Ctag#289", f::Symbol) + r = Ref{var"##Ctag#289"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#289"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#244"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#289"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#245" +struct var"##Ctag#290" data::NTuple{8,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#245"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#290"}, f::Symbol) f === :fence && return Ptr{Ptr{Cvoid}}(x + 0) f === :reserved && return Ptr{Culonglong}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#245", f::Symbol) - r = Ref{var"##Ctag#245"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#245"}, r) +function Base.getproperty(x::var"##Ctag#290", f::Symbol) + r = Ref{var"##Ctag#290"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#290"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#245"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#290"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#245", private::Bool=false) +function Base.propertynames(x::var"##Ctag#290", private::Bool=false) return (:fence, :reserved, if private fieldnames(typeof(x)) else @@ -3179,51 +3179,51 @@ function Base.propertynames(x::var"##Ctag#245", private::Bool=false) end...) end -struct var"##Ctag#246" +struct var"##Ctag#291" key::Culonglong timeoutMs::Cuint end -function Base.getproperty(x::Ptr{var"##Ctag#246"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#291"}, f::Symbol) f === :key && return Ptr{Culonglong}(x + 0) f === :timeoutMs && return Ptr{Cuint}(x + 8) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#246", f::Symbol) - r = Ref{var"##Ctag#246"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#246"}, r) +function Base.getproperty(x::var"##Ctag#291", f::Symbol) + r = Ref{var"##Ctag#291"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#291"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#246"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#291"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#243" +struct var"##Ctag#288" data::NTuple{72,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#243"}, f::Symbol) - f === :fence && return Ptr{var"##Ctag#244"}(x + 0) - f === :nvSciSync && return Ptr{var"##Ctag#245"}(x + 8) - f === :keyedMutex && return Ptr{var"##Ctag#246"}(x + 16) +function Base.getproperty(x::Ptr{var"##Ctag#288"}, f::Symbol) + f === :fence && return Ptr{var"##Ctag#289"}(x + 0) + f === :nvSciSync && return Ptr{var"##Ctag#290"}(x + 8) + f === :keyedMutex && return Ptr{var"##Ctag#291"}(x + 16) f === :reserved && return Ptr{NTuple{10,Cuint}}(x + 32) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#243", f::Symbol) - r = Ref{var"##Ctag#243"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#243"}, r) +function Base.getproperty(x::var"##Ctag#288", f::Symbol) + r = Ref{var"##Ctag#288"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#288"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#243"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#288"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#243", private::Bool=false) +function Base.propertynames(x::var"##Ctag#288", private::Bool=false) return (:fence, :nvSciSync, :keyedMutex, :reserved, if private fieldnames(typeof(x)) else @@ -3374,28 +3374,28 @@ end const CUmemHandleType = CUmemHandleType_enum -struct var"##Ctag#234" +struct var"##Ctag#279" data::NTuple{8,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#234"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#279"}, f::Symbol) f === :mipmap && return Ptr{CUmipmappedArray}(x + 0) f === :array && return Ptr{CUarray}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#234", f::Symbol) - r = Ref{var"##Ctag#234"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#234"}, r) +function Base.getproperty(x::var"##Ctag#279", f::Symbol) + r = Ref{var"##Ctag#279"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#279"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#234"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#279"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#234", private::Bool=false) +function Base.propertynames(x::var"##Ctag#279", private::Bool=false) return (:mipmap, :array, if private fieldnames(typeof(x)) else @@ -3403,28 +3403,28 @@ function Base.propertynames(x::var"##Ctag#234", private::Bool=false) end...) end -struct var"##Ctag#235" +struct var"##Ctag#280" data::NTuple{32,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#235"}, f::Symbol) - f === :sparseLevel && return Ptr{var"##Ctag#236"}(x + 0) - f === :miptail && return Ptr{var"##Ctag#237"}(x + 0) +function Base.getproperty(x::Ptr{var"##Ctag#280"}, f::Symbol) + f === :sparseLevel && return Ptr{var"##Ctag#281"}(x + 0) + f === :miptail && return Ptr{var"##Ctag#282"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#235", f::Symbol) - r = Ref{var"##Ctag#235"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#235"}, r) +function Base.getproperty(x::var"##Ctag#280", f::Symbol) + r = Ref{var"##Ctag#280"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#280"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#235"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#280"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#235", private::Bool=false) +function Base.propertynames(x::var"##Ctag#280", private::Bool=false) return (:sparseLevel, :miptail, if private fieldnames(typeof(x)) else @@ -3432,27 +3432,27 @@ function Base.propertynames(x::var"##Ctag#235", private::Bool=false) end...) end -struct var"##Ctag#238" +struct var"##Ctag#283" data::NTuple{8,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#238"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#283"}, f::Symbol) f === :memHandle && return Ptr{CUmemGenericAllocationHandle}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#238", f::Symbol) - r = Ref{var"##Ctag#238"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#238"}, r) +function Base.getproperty(x::var"##Ctag#283", f::Symbol) + r = Ref{var"##Ctag#283"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#283"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#238"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#283"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#238", private::Bool=false) +function Base.propertynames(x::var"##Ctag#283", private::Bool=false) return (:memHandle, if private fieldnames(typeof(x)) else @@ -3466,12 +3466,12 @@ end function Base.getproperty(x::Ptr{CUarrayMapInfo_st}, f::Symbol) f === :resourceType && return Ptr{CUresourcetype}(x + 0) - f === :resource && return Ptr{var"##Ctag#234"}(x + 8) + f === :resource && return Ptr{var"##Ctag#279"}(x + 8) f === :subresourceType && return Ptr{CUarraySparseSubresourceType}(x + 16) - f === :subresource && return Ptr{var"##Ctag#235"}(x + 24) + f === :subresource && return Ptr{var"##Ctag#280"}(x + 24) f === :memOperationType && return Ptr{CUmemOperationType}(x + 56) f === :memHandleType && return Ptr{CUmemHandleType}(x + 60) - f === :memHandle && return Ptr{var"##Ctag#238"}(x + 64) + f === :memHandle && return Ptr{var"##Ctag#283"}(x + 64) f === :offset && return Ptr{Culonglong}(x + 72) f === :deviceBitMask && return Ptr{Cuint}(x + 80) f === :flags && return Ptr{Cuint}(x + 84) @@ -3511,13 +3511,13 @@ end const CUmemAllocationCompType = CUmemAllocationCompType_enum -struct var"##Ctag#252" +struct var"##Ctag#297" compressionType::Cuchar gpuDirectRDMACapable::Cuchar usage::Cushort reserved::NTuple{4,Cuchar} end -function Base.getproperty(x::Ptr{var"##Ctag#252"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#297"}, f::Symbol) f === :compressionType && return Ptr{Cuchar}(x + 0) f === :gpuDirectRDMACapable && return Ptr{Cuchar}(x + 1) f === :usage && return Ptr{Cushort}(x + 2) @@ -3525,14 +3525,14 @@ function Base.getproperty(x::Ptr{var"##Ctag#252"}, f::Symbol) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#252", f::Symbol) - r = Ref{var"##Ctag#252"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#252"}, r) +function Base.getproperty(x::var"##Ctag#297", f::Symbol) + r = Ref{var"##Ctag#297"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#297"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#252"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#297"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end @@ -3545,7 +3545,7 @@ function Base.getproperty(x::Ptr{CUmemAllocationProp_st}, f::Symbol) f === :requestedHandleTypes && return Ptr{CUmemAllocationHandleType}(x + 4) f === :location && return Ptr{CUmemLocation}(x + 8) f === :win32HandleMetaData && return Ptr{Ptr{Cvoid}}(x + 16) - f === :allocFlags && return Ptr{var"##Ctag#252"}(x + 24) + f === :allocFlags && return Ptr{var"##Ctag#297"}(x + 24) return getfield(x, f) end @@ -6483,28 +6483,28 @@ end @gcsafe_ccall libcuda.cuProfilerStop()::CUresult end -struct var"##Ctag#233" +struct var"##Ctag#278" handle::Ptr{Cvoid} name::Ptr{Cvoid} end -function Base.getproperty(x::Ptr{var"##Ctag#233"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#278"}, f::Symbol) f === :handle && return Ptr{Ptr{Cvoid}}(x + 0) f === :name && return Ptr{Ptr{Cvoid}}(x + 8) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#233", f::Symbol) - r = Ref{var"##Ctag#233"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#233"}, r) +function Base.getproperty(x::var"##Ctag#278", f::Symbol) + r = Ref{var"##Ctag#278"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#278"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#233"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#278"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#236" +struct var"##Ctag#281" level::Cuint layer::Cuint offsetX::Cuint @@ -6514,7 +6514,7 @@ struct var"##Ctag#236" extentHeight::Cuint extentDepth::Cuint end -function Base.getproperty(x::Ptr{var"##Ctag#236"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#281"}, f::Symbol) f === :level && return Ptr{Cuint}(x + 0) f === :layer && return Ptr{Cuint}(x + 4) f === :offsetX && return Ptr{Cuint}(x + 8) @@ -6526,56 +6526,56 @@ function Base.getproperty(x::Ptr{var"##Ctag#236"}, f::Symbol) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#236", f::Symbol) - r = Ref{var"##Ctag#236"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#236"}, r) +function Base.getproperty(x::var"##Ctag#281", f::Symbol) + r = Ref{var"##Ctag#281"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#281"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#236"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#281"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#237" +struct var"##Ctag#282" layer::Cuint offset::Culonglong size::Culonglong end -function Base.getproperty(x::Ptr{var"##Ctag#237"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#282"}, f::Symbol) f === :layer && return Ptr{Cuint}(x + 0) f === :offset && return Ptr{Culonglong}(x + 8) f === :size && return Ptr{Culonglong}(x + 16) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#237", f::Symbol) - r = Ref{var"##Ctag#237"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#237"}, r) +function Base.getproperty(x::var"##Ctag#282", f::Symbol) + r = Ref{var"##Ctag#282"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#282"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#237"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#282"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#240" +struct var"##Ctag#285" bytesOverBudget::Culonglong end -function Base.getproperty(x::Ptr{var"##Ctag#240"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#285"}, f::Symbol) f === :bytesOverBudget && return Ptr{Culonglong}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#240", f::Symbol) - r = Ref{var"##Ctag#240"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#240"}, r) +function Base.getproperty(x::var"##Ctag#285", f::Symbol) + r = Ref{var"##Ctag#285"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#285"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#240"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#285"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end @@ -6657,183 +6657,183 @@ struct CUstreamMemOpMemoryBarrierParams_st flags::Cuint end -struct var"##Ctag#242" +struct var"##Ctag#287" handle::Ptr{Cvoid} name::Ptr{Cvoid} end -function Base.getproperty(x::Ptr{var"##Ctag#242"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#287"}, f::Symbol) f === :handle && return Ptr{Ptr{Cvoid}}(x + 0) f === :name && return Ptr{Ptr{Cvoid}}(x + 8) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#242", f::Symbol) - r = Ref{var"##Ctag#242"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#242"}, r) +function Base.getproperty(x::var"##Ctag#287", f::Symbol) + r = Ref{var"##Ctag#287"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#287"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#242"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#287"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#247" +struct var"##Ctag#292" x::Cuint y::Cuint z::Cuint end -function Base.getproperty(x::Ptr{var"##Ctag#247"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#292"}, f::Symbol) f === :x && return Ptr{Cuint}(x + 0) f === :y && return Ptr{Cuint}(x + 4) f === :z && return Ptr{Cuint}(x + 8) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#247", f::Symbol) - r = Ref{var"##Ctag#247"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#247"}, r) +function Base.getproperty(x::var"##Ctag#292", f::Symbol) + r = Ref{var"##Ctag#292"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#292"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#247"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#292"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#248" +struct var"##Ctag#293" event::CUevent flags::Cint triggerAtBlockStart::Cint end -function Base.getproperty(x::Ptr{var"##Ctag#248"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#293"}, f::Symbol) f === :event && return Ptr{CUevent}(x + 0) f === :flags && return Ptr{Cint}(x + 8) f === :triggerAtBlockStart && return Ptr{Cint}(x + 12) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#248", f::Symbol) - r = Ref{var"##Ctag#248"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#248"}, r) +function Base.getproperty(x::var"##Ctag#293", f::Symbol) + r = Ref{var"##Ctag#293"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#293"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#248"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#293"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#249" +struct var"##Ctag#294" event::CUevent flags::Cint end -function Base.getproperty(x::Ptr{var"##Ctag#249"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#294"}, f::Symbol) f === :event && return Ptr{CUevent}(x + 0) f === :flags && return Ptr{Cint}(x + 8) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#249", f::Symbol) - r = Ref{var"##Ctag#249"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#249"}, r) +function Base.getproperty(x::var"##Ctag#294", f::Symbol) + r = Ref{var"##Ctag#294"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#294"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#249"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#294"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#250" +struct var"##Ctag#295" x::Cuint y::Cuint z::Cuint end -function Base.getproperty(x::Ptr{var"##Ctag#250"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#295"}, f::Symbol) f === :x && return Ptr{Cuint}(x + 0) f === :y && return Ptr{Cuint}(x + 4) f === :z && return Ptr{Cuint}(x + 8) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#250", f::Symbol) - r = Ref{var"##Ctag#250"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#250"}, r) +function Base.getproperty(x::var"##Ctag#295", f::Symbol) + r = Ref{var"##Ctag#295"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#295"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#250"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#295"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#251" +struct var"##Ctag#296" deviceUpdatable::Cint devNode::CUgraphDeviceNode end -function Base.getproperty(x::Ptr{var"##Ctag#251"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#296"}, f::Symbol) f === :deviceUpdatable && return Ptr{Cint}(x + 0) f === :devNode && return Ptr{CUgraphDeviceNode}(x + 8) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#251", f::Symbol) - r = Ref{var"##Ctag#251"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#251"}, r) +function Base.getproperty(x::var"##Ctag#296", f::Symbol) + r = Ref{var"##Ctag#296"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#296"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#251"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#296"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#259" +struct var"##Ctag#304" hArray::CUarray end -function Base.getproperty(x::Ptr{var"##Ctag#259"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#304"}, f::Symbol) f === :hArray && return Ptr{CUarray}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#259", f::Symbol) - r = Ref{var"##Ctag#259"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#259"}, r) +function Base.getproperty(x::var"##Ctag#304", f::Symbol) + r = Ref{var"##Ctag#304"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#304"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#259"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#304"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#260" +struct var"##Ctag#305" hMipmappedArray::CUmipmappedArray end -function Base.getproperty(x::Ptr{var"##Ctag#260"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#305"}, f::Symbol) f === :hMipmappedArray && return Ptr{CUmipmappedArray}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#260", f::Symbol) - r = Ref{var"##Ctag#260"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#260"}, r) +function Base.getproperty(x::var"##Ctag#305", f::Symbol) + r = Ref{var"##Ctag#305"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#305"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#260"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#305"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#261" +struct var"##Ctag#306" devPtr::CUdeviceptr format::CUarray_format numChannels::Cuint sizeInBytes::Csize_t end -function Base.getproperty(x::Ptr{var"##Ctag#261"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#306"}, f::Symbol) f === :devPtr && return Ptr{CUdeviceptr}(x + 0) f === :format && return Ptr{CUarray_format}(x + 8) f === :numChannels && return Ptr{Cuint}(x + 12) @@ -6841,18 +6841,18 @@ function Base.getproperty(x::Ptr{var"##Ctag#261"}, f::Symbol) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#261", f::Symbol) - r = Ref{var"##Ctag#261"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#261"}, r) +function Base.getproperty(x::var"##Ctag#306", f::Symbol) + r = Ref{var"##Ctag#306"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#306"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#261"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#306"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#262" +struct var"##Ctag#307" devPtr::CUdeviceptr format::CUarray_format numChannels::Cuint @@ -6860,7 +6860,7 @@ struct var"##Ctag#262" height::Csize_t pitchInBytes::Csize_t end -function Base.getproperty(x::Ptr{var"##Ctag#262"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#307"}, f::Symbol) f === :devPtr && return Ptr{CUdeviceptr}(x + 0) f === :format && return Ptr{CUarray_format}(x + 8) f === :numChannels && return Ptr{Cuint}(x + 12) @@ -6870,43 +6870,43 @@ function Base.getproperty(x::Ptr{var"##Ctag#262"}, f::Symbol) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#262", f::Symbol) - r = Ref{var"##Ctag#262"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#262"}, r) +function Base.getproperty(x::var"##Ctag#307", f::Symbol) + r = Ref{var"##Ctag#307"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#307"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#262"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#307"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#263" +struct var"##Ctag#308" reserved::NTuple{32,Cint} end -function Base.getproperty(x::Ptr{var"##Ctag#263"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#308"}, f::Symbol) f === :reserved && return Ptr{NTuple{32,Cint}}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#263", f::Symbol) - r = Ref{var"##Ctag#263"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#263"}, r) +function Base.getproperty(x::var"##Ctag#308", f::Symbol) + r = Ref{var"##Ctag#308"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#308"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#263"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#308"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#266" +struct var"##Ctag#311" ptr::CUdeviceptr rowLength::Csize_t layerHeight::Csize_t locHint::CUmemLocation end -function Base.getproperty(x::Ptr{var"##Ctag#266"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#311"}, f::Symbol) f === :ptr && return Ptr{CUdeviceptr}(x + 0) f === :rowLength && return Ptr{Csize_t}(x + 8) f === :layerHeight && return Ptr{Csize_t}(x + 16) @@ -6914,35 +6914,35 @@ function Base.getproperty(x::Ptr{var"##Ctag#266"}, f::Symbol) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#266", f::Symbol) - r = Ref{var"##Ctag#266"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#266"}, r) +function Base.getproperty(x::var"##Ctag#311", f::Symbol) + r = Ref{var"##Ctag#311"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#311"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#266"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#311"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#267" +struct var"##Ctag#312" array::CUarray offset::CUoffset3D end -function Base.getproperty(x::Ptr{var"##Ctag#267"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#312"}, f::Symbol) f === :array && return Ptr{CUarray}(x + 0) f === :offset && return Ptr{CUoffset3D}(x + 8) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#267", f::Symbol) - r = Ref{var"##Ctag#267"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#267"}, r) +function Base.getproperty(x::var"##Ctag#312", f::Symbol) + r = Ref{var"##Ctag#312"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#312"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#267"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#312"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end diff --git a/lib/cudnn/src/libcudnn.jl b/lib/cudnn/src/libcudnn.jl index fc6ff98215..b0978f326b 100644 --- a/lib/cudnn/src/libcudnn.jl +++ b/lib/cudnn/src/libcudnn.jl @@ -170,6 +170,9 @@ end CUDNN_DATA_FAST_FLOAT_FOR_FP8 = 14 CUDNN_DATA_FP8_E8M0 = 15 CUDNN_DATA_FP4_E2M1 = 16 + CUDNN_DATA_INT4 = 17 + CUDNN_DATA_UINT4 = 18 + CUDNN_DATA_UINT32 = 19 end @cenum cudnnMathType_t::UInt32 begin @@ -497,6 +500,7 @@ end CUDNN_ATTR_OPERATION_MATMUL_GEMM_K_OVERRIDE_DESC = 1527 CUDNN_ATTR_REDUCTION_OPERATOR = 1600 CUDNN_ATTR_REDUCTION_COMP_TYPE = 1601 + CUDNN_ATTR_REDUCTION_IS_DETERMINISTIC = 1602 CUDNN_ATTR_OPERATION_REDUCTION_XDESC = 1610 CUDNN_ATTR_OPERATION_REDUCTION_YDESC = 1611 CUDNN_ATTR_OPERATION_REDUCTION_DESC = 1612 @@ -582,6 +586,7 @@ end CUDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_AXIS = 2254 CUDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_PAD_VALUE = 2255 CUDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_KV_TOKEN_OFFSET_DESC = 2256 + CUDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_SPECULATIVE_MASK_DESC = 2257 CUDNN_ATTR_OPERATION_CONTRACT_BAND_MATRIX_XDESC = 2270 CUDNN_ATTR_OPERATION_CONTRACT_BAND_MATRIX_YDESC = 2271 CUDNN_ATTR_OPERATION_CONTRACT_BAND_MATRIX_LOWER_BANDWIDTH = 2272 @@ -612,9 +617,16 @@ end CUDNN_ATTR_OPERATION_BLOCK_SCALE_DEQUANTIZE_YDESC = 2602 CUDNN_ATTR_OPERATION_BLOCK_SCALE_DEQUANTIZE_MATH_PREC = 2603 CUDNN_ATTR_OPERATION_BLOCK_SCALE_DEQUANTIZE_BLOCK_SIZE = 2604 + CUDNN_ATTR_OPERATION_BLOCK_SCALE_DEQUANTIZE_NEG_SCALE = 2605 CUDNN_ATTR_DEVICEPROP_DEVICE_ID = 2700 CUDNN_ATTR_DEVICEPROP_HANDLE = 2701 CUDNN_ATTR_DEVICEPROP_JSON_REPRESENTATION = 2702 + CUDNN_ATTR_OPERATION_SDPA_FWD_QDESC = 2800 + CUDNN_ATTR_OPERATION_SDPA_FWD_KDESC = 2801 + CUDNN_ATTR_OPERATION_SDPA_FWD_VDESC = 2802 + CUDNN_ATTR_OPERATION_SDPA_FWD_ODESC = 2803 + CUDNN_ATTR_OPERATION_SDPA_FWD_STATSDESC = 2804 + CUDNN_ATTR_OPERATION_SDPA_FWD_SCALEDESC = 2805 end @cenum cudnnBackendAttributeType_t::UInt32 begin @@ -687,11 +699,12 @@ end CUDNN_BACKEND_OPERATION_RNG_DESCRIPTOR = 33 CUDNN_BACKEND_KERNEL_CACHE_DESCRIPTOR = 34 CUDNN_BACKEND_OPERATION_PAGED_CACHE_LOAD_DESCRIPTOR = 35 - CUDNN_BACKEND_OPERATION_EXPAND_BAND_MATRIX_DESCRIPTOR = 36 - CUDNN_BACKEND_OPERATION_CONTRACT_BAND_MATRIX_DESCRIPTOR = 37 - CUDNN_BACKEND_OPERATION_BLOCK_SCALE_QUANTIZE_DESCRIPTOR = 38 - CUDNN_BACKEND_OPERATION_BLOCK_SCALE_DEQUANTIZE_DESCRIPTOR = 39 - CUDNN_BACKEND_DEVICEPROP_DESCRIPTOR = 40 + CUDNN_BACKEND_OPERATION_BLOCK_SCALE_QUANTIZE_DESCRIPTOR = 36 + CUDNN_BACKEND_OPERATION_BLOCK_SCALE_DEQUANTIZE_DESCRIPTOR = 37 + CUDNN_BACKEND_DEVICEPROP_DESCRIPTOR = 38 + CUDNN_BACKEND_OPERATION_EXPAND_BAND_MATRIX_DESCRIPTOR = 39 + CUDNN_BACKEND_OPERATION_CONTRACT_BAND_MATRIX_DESCRIPTOR = 40 + CUDNN_BACKEND_OPERATION_SDPA_FWD_DESCRIPTOR = 41 end @cenum cudnnBackendNumericalNote_t::UInt32 begin @@ -3611,7 +3624,7 @@ end const CUDNN_MAX_SM_MAJOR_NUMBER = 12 -const CUDNN_MAX_SM_MINOR_NUMBER = 0 +const CUDNN_MAX_SM_MINOR_NUMBER = 1 const CUDNN_DIM_MAX = 8 diff --git a/lib/cupti/libcupti.jl b/lib/cupti/libcupti.jl index 4a4e745035..901b470a2b 100644 --- a/lib/cupti/libcupti.jl +++ b/lib/cupti/libcupti.jl @@ -192,27 +192,27 @@ struct CUpti_CallbackData correlationId::UInt32 end -struct var"##Ctag#380" +struct var"##Ctag#425" data::NTuple{8,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#380"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#425"}, f::Symbol) f === :stream && return Ptr{CUstream}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#380", f::Symbol) - r = Ref{var"##Ctag#380"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#380"}, r) +function Base.getproperty(x::var"##Ctag#425", f::Symbol) + r = Ref{var"##Ctag#425"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#425"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#380"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#425"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#380", private::Bool=false) +function Base.propertynames(x::var"##Ctag#425", private::Bool=false) return (:stream, if private fieldnames(typeof(x)) else @@ -226,7 +226,7 @@ end function Base.getproperty(x::Ptr{CUpti_ResourceData}, f::Symbol) f === :context && return Ptr{CUcontext}(x + 0) - f === :resourceHandle && return Ptr{var"##Ctag#380"}(x + 8) + f === :resourceHandle && return Ptr{var"##Ctag#425"}(x + 8) f === :resourceDescriptor && return Ptr{Ptr{Cvoid}}(x + 16) return getfield(x, f) end @@ -1000,8 +1000,8 @@ struct CUpti_ActivityObjectKindId end function Base.getproperty(x::Ptr{CUpti_ActivityObjectKindId}, f::Symbol) - f === :pt && return Ptr{var"##Ctag#396"}(x + 0) - f === :dcs && return Ptr{var"##Ctag#397"}(x + 0) + f === :pt && return Ptr{var"##Ctag#441"}(x + 0) + f === :dcs && return Ptr{var"##Ctag#442"}(x + 0) return getfield(x, f) end @@ -1633,28 +1633,28 @@ function Base.propertynames(x::CUpti_ActivityMemory, private::Bool=false) end...) end -struct var"##Ctag#309" +struct var"##Ctag#354" data::NTuple{8,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#309"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#354"}, f::Symbol) f === :size && return Ptr{UInt64}(x + 0) f === :processId && return Ptr{UInt64}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#309", f::Symbol) - r = Ref{var"##Ctag#309"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#309"}, r) +function Base.getproperty(x::var"##Ctag#354", f::Symbol) + r = Ref{var"##Ctag#354"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#354"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#309"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#354"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#309", private::Bool=false) +function Base.propertynames(x::var"##Ctag#354", private::Bool=false) return (:size, :processId, if private fieldnames(typeof(x)) else @@ -1662,32 +1662,32 @@ function Base.propertynames(x::var"##Ctag#309", private::Bool=false) end...) end -struct var"##Ctag#308" +struct var"##Ctag#353" data::NTuple{40,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#308"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#353"}, f::Symbol) f === :memoryPoolType && return Ptr{CUpti_ActivityMemoryPoolType}(x + 0) f === :pad2 && return Ptr{UInt32}(x + 4) f === :address && return Ptr{UInt64}(x + 8) f === :releaseThreshold && return Ptr{UInt64}(x + 16) - f === :pool && return Ptr{var"##Ctag#309"}(x + 24) + f === :pool && return Ptr{var"##Ctag#354"}(x + 24) f === :utilizedSize && return Ptr{UInt64}(x + 32) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#308", f::Symbol) - r = Ref{var"##Ctag#308"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#308"}, r) +function Base.getproperty(x::var"##Ctag#353", f::Symbol) + r = Ref{var"##Ctag#353"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#353"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#308"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#353"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#308", private::Bool=false) +function Base.propertynames(x::var"##Ctag#353", private::Bool=false) return (:memoryPoolType, :pad2, :address, :releaseThreshold, :pool, :utilizedSize, if private fieldnames(typeof(x)) @@ -1799,28 +1799,28 @@ end CUPTI_FUNC_SHMEM_LIMIT_FORCE_INT = 2147483647 end -struct var"##Ctag#346" +struct var"##Ctag#391" data::NTuple{1,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#346"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#391"}, f::Symbol) f === :both && return Ptr{UInt8}(x + 0) - f === :config && return Ptr{var"##Ctag#347"}(x + 0) + f === :config && return Ptr{var"##Ctag#392"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#346", f::Symbol) - r = Ref{var"##Ctag#346"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#346"}, r) +function Base.getproperty(x::var"##Ctag#391", f::Symbol) + r = Ref{var"##Ctag#391"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#391"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#346"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#391"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#346", private::Bool=false) +function Base.propertynames(x::var"##Ctag#391", private::Bool=false) return (:both, :config, if private fieldnames(typeof(x)) else @@ -1834,7 +1834,7 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityKernel10}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) - f === :cacheConfig && return Ptr{var"##Ctag#346"}(x + 4) + f === :cacheConfig && return Ptr{var"##Ctag#391"}(x + 4) f === :sharedMemoryConfig && return Ptr{UInt8}(x + 5) f === :registersPerThread && return Ptr{UInt16}(x + 6) f === :partitionedGlobalCacheRequested && @@ -1915,28 +1915,28 @@ function Base.propertynames(x::CUpti_ActivityKernel10, private::Bool=false) end...) end -struct var"##Ctag#306" +struct var"##Ctag#351" data::NTuple{1,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#306"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#351"}, f::Symbol) f === :both && return Ptr{UInt8}(x + 0) - f === :config && return Ptr{var"##Ctag#307"}(x + 0) + f === :config && return Ptr{var"##Ctag#352"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#306", f::Symbol) - r = Ref{var"##Ctag#306"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#306"}, r) +function Base.getproperty(x::var"##Ctag#351", f::Symbol) + r = Ref{var"##Ctag#351"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#351"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#306"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#351"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#306", private::Bool=false) +function Base.propertynames(x::var"##Ctag#351", private::Bool=false) return (:both, :config, if private fieldnames(typeof(x)) else @@ -1950,7 +1950,7 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityCdpKernel}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) - f === :cacheConfig && return Ptr{var"##Ctag#306"}(x + 4) + f === :cacheConfig && return Ptr{var"##Ctag#351"}(x + 4) f === :sharedMemoryConfig && return Ptr{UInt8}(x + 5) f === :registersPerThread && return Ptr{UInt16}(x + 6) f === :start && return Ptr{UInt64}(x + 8) @@ -2395,28 +2395,28 @@ function Base.propertynames(x::CUpti_ActivityDevice5, private::Bool=false) end...) end -struct var"##Ctag#366" +struct var"##Ctag#411" data::NTuple{4,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#366"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#411"}, f::Symbol) f === :cu && return Ptr{CUdevice_attribute}(x + 0) f === :cupti && return Ptr{CUpti_DeviceAttribute}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#366", f::Symbol) - r = Ref{var"##Ctag#366"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#366"}, r) +function Base.getproperty(x::var"##Ctag#411", f::Symbol) + r = Ref{var"##Ctag#411"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#411"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#366"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#411"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#366", private::Bool=false) +function Base.propertynames(x::var"##Ctag#411", private::Bool=false) return (:cu, :cupti, if private fieldnames(typeof(x)) else @@ -2424,11 +2424,11 @@ function Base.propertynames(x::var"##Ctag#366", private::Bool=false) end...) end -struct var"##Ctag#367" +struct var"##Ctag#412" data::NTuple{8,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#367"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#412"}, f::Symbol) f === :vDouble && return Ptr{Cdouble}(x + 0) f === :vUint32 && return Ptr{UInt32}(x + 0) f === :vUint64 && return Ptr{UInt64}(x + 0) @@ -2437,18 +2437,18 @@ function Base.getproperty(x::Ptr{var"##Ctag#367"}, f::Symbol) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#367", f::Symbol) - r = Ref{var"##Ctag#367"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#367"}, r) +function Base.getproperty(x::var"##Ctag#412", f::Symbol) + r = Ref{var"##Ctag#412"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#412"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#367"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#412"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#367", private::Bool=false) +function Base.propertynames(x::var"##Ctag#412", private::Bool=false) return (:vDouble, :vUint32, :vUint64, :vInt32, :vInt64, if private fieldnames(typeof(x)) else @@ -2464,8 +2464,8 @@ function Base.getproperty(x::Ptr{CUpti_ActivityDeviceAttribute}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) f === :flags && return Ptr{CUpti_ActivityFlag}(x + 4) f === :deviceId && return Ptr{UInt32}(x + 8) - f === :attribute && return Ptr{var"##Ctag#366"}(x + 12) - f === :value && return Ptr{var"##Ctag#367"}(x + 16) + f === :attribute && return Ptr{var"##Ctag#411"}(x + 12) + f === :value && return Ptr{var"##Ctag#412"}(x + 16) return getfield(x, f) end @@ -2671,30 +2671,30 @@ function Base.propertynames(x::CUpti_ActivityOverhead3, private::Bool=false) end...) end -struct var"##Ctag#355" +struct var"##Ctag#400" data::NTuple{20,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#355"}, f::Symbol) - f === :speed && return Ptr{var"##Ctag#356"}(x + 0) - f === :temperature && return Ptr{var"##Ctag#357"}(x + 0) - f === :power && return Ptr{var"##Ctag#358"}(x + 0) - f === :cooling && return Ptr{var"##Ctag#359"}(x + 0) +function Base.getproperty(x::Ptr{var"##Ctag#400"}, f::Symbol) + f === :speed && return Ptr{var"##Ctag#401"}(x + 0) + f === :temperature && return Ptr{var"##Ctag#402"}(x + 0) + f === :power && return Ptr{var"##Ctag#403"}(x + 0) + f === :cooling && return Ptr{var"##Ctag#404"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#355", f::Symbol) - r = Ref{var"##Ctag#355"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#355"}, r) +function Base.getproperty(x::var"##Ctag#400", f::Symbol) + r = Ref{var"##Ctag#400"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#400"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#355"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#400"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#355", private::Bool=false) +function Base.propertynames(x::var"##Ctag#400", private::Bool=false) return (:speed, :temperature, :power, :cooling, if private fieldnames(typeof(x)) else @@ -2711,7 +2711,7 @@ function Base.getproperty(x::Ptr{CUpti_ActivityEnvironment}, f::Symbol) f === :deviceId && return Ptr{UInt32}(x + 4) f === :timestamp && return Ptr{UInt64}(x + 8) f === :environmentKind && return Ptr{CUpti_ActivityEnvironmentKind}(x + 16) - f === :data && return Ptr{var"##Ctag#355"}(x + 20) + f === :data && return Ptr{var"##Ctag#400"}(x + 20) return getfield(x, f) end @@ -3507,28 +3507,28 @@ end CUPTI_DEV_TYPE_FORCE_INT = 2147483647 end -struct var"##Ctag#348" +struct var"##Ctag#393" data::NTuple{16,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#348"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#393"}, f::Symbol) f === :uuidDev && return Ptr{CUuuid}(x + 0) - f === :npu && return Ptr{var"##Ctag#349"}(x + 0) + f === :npu && return Ptr{var"##Ctag#394"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#348", f::Symbol) - r = Ref{var"##Ctag#348"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#348"}, r) +function Base.getproperty(x::var"##Ctag#393", f::Symbol) + r = Ref{var"##Ctag#393"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#393"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#348"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#393"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#348", private::Bool=false) +function Base.propertynames(x::var"##Ctag#393", private::Bool=false) return (:uuidDev, :npu, if private fieldnames(typeof(x)) else @@ -3536,28 +3536,28 @@ function Base.propertynames(x::var"##Ctag#348", private::Bool=false) end...) end -struct var"##Ctag#350" +struct var"##Ctag#395" data::NTuple{16,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#350"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#395"}, f::Symbol) f === :uuidDev && return Ptr{CUuuid}(x + 0) - f === :npu && return Ptr{var"##Ctag#351"}(x + 0) + f === :npu && return Ptr{var"##Ctag#396"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#350", f::Symbol) - r = Ref{var"##Ctag#350"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#350"}, r) +function Base.getproperty(x::var"##Ctag#395", f::Symbol) + r = Ref{var"##Ctag#395"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#395"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#350"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#395"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#350", private::Bool=false) +function Base.propertynames(x::var"##Ctag#395", private::Bool=false) return (:uuidDev, :npu, if private fieldnames(typeof(x)) else @@ -3574,8 +3574,8 @@ function Base.getproperty(x::Ptr{CUpti_ActivityNvLink4}, f::Symbol) f === :nvlinkVersion && return Ptr{UInt32}(x + 4) f === :typeDev0 && return Ptr{CUpti_DevType}(x + 8) f === :typeDev1 && return Ptr{CUpti_DevType}(x + 12) - f === :idDev0 && return Ptr{var"##Ctag#348"}(x + 16) - f === :idDev1 && return Ptr{var"##Ctag#350"}(x + 32) + f === :idDev0 && return Ptr{var"##Ctag#393"}(x + 16) + f === :idDev1 && return Ptr{var"##Ctag#395"}(x + 32) f === :flag && return Ptr{UInt32}(x + 48) f === :physicalNvLinkCount && return Ptr{UInt32}(x + 52) f === :portDev0 && return Ptr{NTuple{32,Int8}}(x + 56) @@ -3613,28 +3613,28 @@ end CUPTI_PCIE_DEVICE_TYPE_FORCE_INT = 2147483647 end -struct var"##Ctag#360" +struct var"##Ctag#405" data::NTuple{4,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#360"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#405"}, f::Symbol) f === :devId && return Ptr{CUdevice}(x + 0) f === :bridgeId && return Ptr{UInt32}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#360", f::Symbol) - r = Ref{var"##Ctag#360"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#360"}, r) +function Base.getproperty(x::var"##Ctag#405", f::Symbol) + r = Ref{var"##Ctag#405"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#405"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#360"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#405"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#360", private::Bool=false) +function Base.propertynames(x::var"##Ctag#405", private::Bool=false) return (:devId, :bridgeId, if private fieldnames(typeof(x)) else @@ -3642,28 +3642,28 @@ function Base.propertynames(x::var"##Ctag#360", private::Bool=false) end...) end -struct var"##Ctag#361" +struct var"##Ctag#406" data::NTuple{144,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#361"}, f::Symbol) - f === :gpuAttr && return Ptr{var"##Ctag#362"}(x + 0) - f === :bridgeAttr && return Ptr{var"##Ctag#363"}(x + 0) +function Base.getproperty(x::Ptr{var"##Ctag#406"}, f::Symbol) + f === :gpuAttr && return Ptr{var"##Ctag#407"}(x + 0) + f === :bridgeAttr && return Ptr{var"##Ctag#408"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#361", f::Symbol) - r = Ref{var"##Ctag#361"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#361"}, r) +function Base.getproperty(x::var"##Ctag#406", f::Symbol) + r = Ref{var"##Ctag#406"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#406"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#361"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#406"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#361", private::Bool=false) +function Base.propertynames(x::var"##Ctag#406", private::Bool=false) return (:gpuAttr, :bridgeAttr, if private fieldnames(typeof(x)) else @@ -3678,13 +3678,13 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityPcie}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) f === :type && return Ptr{CUpti_PcieDeviceType}(x + 4) - f === :id && return Ptr{var"##Ctag#360"}(x + 8) + f === :id && return Ptr{var"##Ctag#405"}(x + 8) f === :domain && return Ptr{UInt32}(x + 12) f === :pcieGeneration && return Ptr{UInt16}(x + 16) f === :linkRate && return Ptr{UInt16}(x + 18) f === :linkWidth && return Ptr{UInt16}(x + 20) f === :upstreamBus && return Ptr{UInt16}(x + 22) - f === :attr && return Ptr{var"##Ctag#361"}(x + 24) + f === :attr && return Ptr{var"##Ctag#406"}(x + 24) return getfield(x, f) end @@ -4679,28 +4679,28 @@ function Base.propertynames(x::CUpti_ActivityKernel, private::Bool=false) end...) end -struct var"##Ctag#364" +struct var"##Ctag#409" data::NTuple{1,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#364"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#409"}, f::Symbol) f === :both && return Ptr{UInt8}(x + 0) - f === :config && return Ptr{var"##Ctag#365"}(x + 0) + f === :config && return Ptr{var"##Ctag#410"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#364", f::Symbol) - r = Ref{var"##Ctag#364"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#364"}, r) +function Base.getproperty(x::var"##Ctag#409", f::Symbol) + r = Ref{var"##Ctag#409"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#409"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#364"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#409"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#364", private::Bool=false) +function Base.propertynames(x::var"##Ctag#409", private::Bool=false) return (:both, :config, if private fieldnames(typeof(x)) else @@ -4714,7 +4714,7 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityKernel2}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) - f === :cacheConfig && return Ptr{var"##Ctag#364"}(x + 4) + f === :cacheConfig && return Ptr{var"##Ctag#409"}(x + 4) f === :sharedMemoryConfig && return Ptr{UInt8}(x + 5) f === :registersPerThread && return Ptr{UInt16}(x + 6) f === :start && return Ptr{UInt64}(x + 8) @@ -4763,28 +4763,28 @@ function Base.propertynames(x::CUpti_ActivityKernel2, private::Bool=false) end...) end -struct var"##Ctag#287" +struct var"##Ctag#332" data::NTuple{1,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#287"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#332"}, f::Symbol) f === :both && return Ptr{UInt8}(x + 0) - f === :config && return Ptr{var"##Ctag#288"}(x + 0) + f === :config && return Ptr{var"##Ctag#333"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#287", f::Symbol) - r = Ref{var"##Ctag#287"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#287"}, r) +function Base.getproperty(x::var"##Ctag#332", f::Symbol) + r = Ref{var"##Ctag#332"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#332"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#287"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#332"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#287", private::Bool=false) +function Base.propertynames(x::var"##Ctag#332", private::Bool=false) return (:both, :config, if private fieldnames(typeof(x)) else @@ -4798,7 +4798,7 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityKernel3}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) - f === :cacheConfig && return Ptr{var"##Ctag#287"}(x + 4) + f === :cacheConfig && return Ptr{var"##Ctag#332"}(x + 4) f === :sharedMemoryConfig && return Ptr{UInt8}(x + 5) f === :registersPerThread && return Ptr{UInt16}(x + 6) f === :partitionedGlobalCacheRequested && @@ -4852,28 +4852,28 @@ function Base.propertynames(x::CUpti_ActivityKernel3, private::Bool=false) end...) end -struct var"##Ctag#310" +struct var"##Ctag#355" data::NTuple{1,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#310"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#355"}, f::Symbol) f === :both && return Ptr{UInt8}(x + 0) - f === :config && return Ptr{var"##Ctag#311"}(x + 0) + f === :config && return Ptr{var"##Ctag#356"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#310", f::Symbol) - r = Ref{var"##Ctag#310"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#310"}, r) +function Base.getproperty(x::var"##Ctag#355", f::Symbol) + r = Ref{var"##Ctag#355"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#355"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#310"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#355"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#310", private::Bool=false) +function Base.propertynames(x::var"##Ctag#355", private::Bool=false) return (:both, :config, if private fieldnames(typeof(x)) else @@ -4887,7 +4887,7 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityKernel4}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) - f === :cacheConfig && return Ptr{var"##Ctag#310"}(x + 4) + f === :cacheConfig && return Ptr{var"##Ctag#355"}(x + 4) f === :sharedMemoryConfig && return Ptr{UInt8}(x + 5) f === :registersPerThread && return Ptr{UInt16}(x + 6) f === :partitionedGlobalCacheRequested && @@ -4950,28 +4950,28 @@ function Base.propertynames(x::CUpti_ActivityKernel4, private::Bool=false) end...) end -struct var"##Ctag#344" +struct var"##Ctag#389" data::NTuple{1,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#344"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#389"}, f::Symbol) f === :both && return Ptr{UInt8}(x + 0) - f === :config && return Ptr{var"##Ctag#345"}(x + 0) + f === :config && return Ptr{var"##Ctag#390"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#344", f::Symbol) - r = Ref{var"##Ctag#344"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#344"}, r) +function Base.getproperty(x::var"##Ctag#389", f::Symbol) + r = Ref{var"##Ctag#389"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#389"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#344"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#389"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#344", private::Bool=false) +function Base.propertynames(x::var"##Ctag#389", private::Bool=false) return (:both, :config, if private fieldnames(typeof(x)) else @@ -4985,7 +4985,7 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityKernel5}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) - f === :cacheConfig && return Ptr{var"##Ctag#344"}(x + 4) + f === :cacheConfig && return Ptr{var"##Ctag#389"}(x + 4) f === :sharedMemoryConfig && return Ptr{UInt8}(x + 5) f === :registersPerThread && return Ptr{UInt16}(x + 6) f === :partitionedGlobalCacheRequested && @@ -5051,28 +5051,28 @@ function Base.propertynames(x::CUpti_ActivityKernel5, private::Bool=false) end...) end -struct var"##Ctag#291" +struct var"##Ctag#336" data::NTuple{1,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#291"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#336"}, f::Symbol) f === :both && return Ptr{UInt8}(x + 0) - f === :config && return Ptr{var"##Ctag#292"}(x + 0) + f === :config && return Ptr{var"##Ctag#337"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#291", f::Symbol) - r = Ref{var"##Ctag#291"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#291"}, r) +function Base.getproperty(x::var"##Ctag#336", f::Symbol) + r = Ref{var"##Ctag#336"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#336"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#291"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#336"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#291", private::Bool=false) +function Base.propertynames(x::var"##Ctag#336", private::Bool=false) return (:both, :config, if private fieldnames(typeof(x)) else @@ -5086,7 +5086,7 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityKernel6}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) - f === :cacheConfig && return Ptr{var"##Ctag#291"}(x + 4) + f === :cacheConfig && return Ptr{var"##Ctag#336"}(x + 4) f === :sharedMemoryConfig && return Ptr{UInt8}(x + 5) f === :registersPerThread && return Ptr{UInt16}(x + 6) f === :partitionedGlobalCacheRequested && @@ -5153,28 +5153,28 @@ function Base.propertynames(x::CUpti_ActivityKernel6, private::Bool=false) end...) end -struct var"##Ctag#294" +struct var"##Ctag#339" data::NTuple{1,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#294"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#339"}, f::Symbol) f === :both && return Ptr{UInt8}(x + 0) - f === :config && return Ptr{var"##Ctag#295"}(x + 0) + f === :config && return Ptr{var"##Ctag#340"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#294", f::Symbol) - r = Ref{var"##Ctag#294"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#294"}, r) +function Base.getproperty(x::var"##Ctag#339", f::Symbol) + r = Ref{var"##Ctag#339"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#339"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#294"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#339"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#294", private::Bool=false) +function Base.propertynames(x::var"##Ctag#339", private::Bool=false) return (:both, :config, if private fieldnames(typeof(x)) else @@ -5188,7 +5188,7 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityKernel7}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) - f === :cacheConfig && return Ptr{var"##Ctag#294"}(x + 4) + f === :cacheConfig && return Ptr{var"##Ctag#339"}(x + 4) f === :sharedMemoryConfig && return Ptr{UInt8}(x + 5) f === :registersPerThread && return Ptr{UInt16}(x + 6) f === :partitionedGlobalCacheRequested && @@ -5258,28 +5258,28 @@ function Base.propertynames(x::CUpti_ActivityKernel7, private::Bool=false) end...) end -struct var"##Ctag#378" +struct var"##Ctag#423" data::NTuple{1,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#378"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#423"}, f::Symbol) f === :both && return Ptr{UInt8}(x + 0) - f === :config && return Ptr{var"##Ctag#379"}(x + 0) + f === :config && return Ptr{var"##Ctag#424"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#378", f::Symbol) - r = Ref{var"##Ctag#378"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#378"}, r) +function Base.getproperty(x::var"##Ctag#423", f::Symbol) + r = Ref{var"##Ctag#423"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#423"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#378"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#423"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#378", private::Bool=false) +function Base.propertynames(x::var"##Ctag#423", private::Bool=false) return (:both, :config, if private fieldnames(typeof(x)) else @@ -5293,7 +5293,7 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityKernel8}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) - f === :cacheConfig && return Ptr{var"##Ctag#378"}(x + 4) + f === :cacheConfig && return Ptr{var"##Ctag#423"}(x + 4) f === :sharedMemoryConfig && return Ptr{UInt8}(x + 5) f === :registersPerThread && return Ptr{UInt16}(x + 6) f === :partitionedGlobalCacheRequested && @@ -5369,28 +5369,28 @@ function Base.propertynames(x::CUpti_ActivityKernel8, private::Bool=false) end...) end -struct var"##Ctag#353" +struct var"##Ctag#398" data::NTuple{1,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#353"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#398"}, f::Symbol) f === :both && return Ptr{UInt8}(x + 0) - f === :config && return Ptr{var"##Ctag#354"}(x + 0) + f === :config && return Ptr{var"##Ctag#399"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#353", f::Symbol) - r = Ref{var"##Ctag#353"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#353"}, r) +function Base.getproperty(x::var"##Ctag#398", f::Symbol) + r = Ref{var"##Ctag#398"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#398"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#353"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#398"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#353", private::Bool=false) +function Base.propertynames(x::var"##Ctag#398", private::Bool=false) return (:both, :config, if private fieldnames(typeof(x)) else @@ -5404,7 +5404,7 @@ end function Base.getproperty(x::Ptr{CUpti_ActivityKernel9}, f::Symbol) f === :kind && return Ptr{CUpti_ActivityKind}(x + 0) - f === :cacheConfig && return Ptr{var"##Ctag#353"}(x + 4) + f === :cacheConfig && return Ptr{var"##Ctag#398"}(x + 4) f === :sharedMemoryConfig && return Ptr{UInt8}(x + 5) f === :registersPerThread && return Ptr{UInt16}(x + 6) f === :partitionedGlobalCacheRequested && @@ -5893,28 +5893,28 @@ function Base.propertynames(x::CUpti_ActivityMemset3, private::Bool=false) end...) end -struct var"##Ctag#331" +struct var"##Ctag#376" data::NTuple{8,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#331"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#376"}, f::Symbol) f === :size && return Ptr{UInt64}(x + 0) f === :processId && return Ptr{UInt64}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#331", f::Symbol) - r = Ref{var"##Ctag#331"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#331"}, r) +function Base.getproperty(x::var"##Ctag#376", f::Symbol) + r = Ref{var"##Ctag#376"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#376"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#331"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#376"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#331", private::Bool=false) +function Base.propertynames(x::var"##Ctag#376", private::Bool=false) return (:size, :processId, if private fieldnames(typeof(x)) else @@ -5922,31 +5922,31 @@ function Base.propertynames(x::var"##Ctag#331", private::Bool=false) end...) end -struct var"##Ctag#330" +struct var"##Ctag#375" data::NTuple{32,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#330"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#375"}, f::Symbol) f === :memoryPoolType && return Ptr{CUpti_ActivityMemoryPoolType}(x + 0) f === :pad2 && return Ptr{UInt32}(x + 4) f === :address && return Ptr{UInt64}(x + 8) f === :releaseThreshold && return Ptr{UInt64}(x + 16) - f === :pool && return Ptr{var"##Ctag#331"}(x + 24) + f === :pool && return Ptr{var"##Ctag#376"}(x + 24) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#330", f::Symbol) - r = Ref{var"##Ctag#330"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#330"}, r) +function Base.getproperty(x::var"##Ctag#375", f::Symbol) + r = Ref{var"##Ctag#375"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#375"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#330"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#375"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#330", private::Bool=false) +function Base.propertynames(x::var"##Ctag#375", private::Bool=false) return (:memoryPoolType, :pad2, :address, :releaseThreshold, :pool, if private fieldnames(typeof(x)) @@ -6000,28 +6000,28 @@ function Base.propertynames(x::CUpti_ActivityMemory2, private::Bool=false) end...) end -struct var"##Ctag#315" +struct var"##Ctag#360" data::NTuple{8,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#315"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#360"}, f::Symbol) f === :size && return Ptr{UInt64}(x + 0) f === :processId && return Ptr{UInt64}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#315", f::Symbol) - r = Ref{var"##Ctag#315"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#315"}, r) +function Base.getproperty(x::var"##Ctag#360", f::Symbol) + r = Ref{var"##Ctag#360"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#360"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#315"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#360"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#315", private::Bool=false) +function Base.propertynames(x::var"##Ctag#360", private::Bool=false) return (:size, :processId, if private fieldnames(typeof(x)) else @@ -6029,32 +6029,32 @@ function Base.propertynames(x::var"##Ctag#315", private::Bool=false) end...) end -struct var"##Ctag#314" +struct var"##Ctag#359" data::NTuple{40,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#314"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#359"}, f::Symbol) f === :memoryPoolType && return Ptr{CUpti_ActivityMemoryPoolType}(x + 0) f === :pad2 && return Ptr{UInt32}(x + 4) f === :address && return Ptr{UInt64}(x + 8) f === :releaseThreshold && return Ptr{UInt64}(x + 16) - f === :pool && return Ptr{var"##Ctag#315"}(x + 24) + f === :pool && return Ptr{var"##Ctag#360"}(x + 24) f === :utilizedSize && return Ptr{UInt64}(x + 32) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#314", f::Symbol) - r = Ref{var"##Ctag#314"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#314"}, r) +function Base.getproperty(x::var"##Ctag#359", f::Symbol) + r = Ref{var"##Ctag#359"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#359"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#314"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#359"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#314", private::Bool=false) +function Base.propertynames(x::var"##Ctag#359", private::Bool=false) return (:memoryPoolType, :pad2, :address, :releaseThreshold, :pool, :utilizedSize, if private fieldnames(typeof(x)) @@ -6488,28 +6488,28 @@ function Base.propertynames(x::CUpti_ActivityUnifiedMemoryCounter2, private::Boo end...) end -struct var"##Ctag#275" +struct var"##Ctag#320" data::NTuple{16,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#275"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#320"}, f::Symbol) f === :uuidDev && return Ptr{CUuuid}(x + 0) - f === :npu && return Ptr{var"##Ctag#276"}(x + 0) + f === :npu && return Ptr{var"##Ctag#321"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#275", f::Symbol) - r = Ref{var"##Ctag#275"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#275"}, r) +function Base.getproperty(x::var"##Ctag#320", f::Symbol) + r = Ref{var"##Ctag#320"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#320"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#275"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#320"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#275", private::Bool=false) +function Base.propertynames(x::var"##Ctag#320", private::Bool=false) return (:uuidDev, :npu, if private fieldnames(typeof(x)) else @@ -6517,28 +6517,28 @@ function Base.propertynames(x::var"##Ctag#275", private::Bool=false) end...) end -struct var"##Ctag#277" +struct var"##Ctag#322" data::NTuple{16,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#277"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#322"}, f::Symbol) f === :uuidDev && return Ptr{CUuuid}(x + 0) - f === :npu && return Ptr{var"##Ctag#278"}(x + 0) + f === :npu && return Ptr{var"##Ctag#323"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#277", f::Symbol) - r = Ref{var"##Ctag#277"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#277"}, r) +function Base.getproperty(x::var"##Ctag#322", f::Symbol) + r = Ref{var"##Ctag#322"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#322"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#277"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#322"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#277", private::Bool=false) +function Base.propertynames(x::var"##Ctag#322", private::Bool=false) return (:uuidDev, :npu, if private fieldnames(typeof(x)) else @@ -6555,8 +6555,8 @@ function Base.getproperty(x::Ptr{CUpti_ActivityNvLink}, f::Symbol) f === :nvlinkVersion && return Ptr{UInt32}(x + 4) f === :typeDev0 && return Ptr{CUpti_DevType}(x + 8) f === :typeDev1 && return Ptr{CUpti_DevType}(x + 12) - f === :idDev0 && return Ptr{var"##Ctag#275"}(x + 16) - f === :idDev1 && return Ptr{var"##Ctag#277"}(x + 32) + f === :idDev0 && return Ptr{var"##Ctag#320"}(x + 16) + f === :idDev1 && return Ptr{var"##Ctag#322"}(x + 32) f === :flag && return Ptr{UInt32}(x + 48) f === :physicalNvLinkCount && return Ptr{UInt32}(x + 52) f === :portDev0 && return Ptr{NTuple{4,Int8}}(x + 56) @@ -6586,28 +6586,28 @@ function Base.propertynames(x::CUpti_ActivityNvLink, private::Bool=false) end...) end -struct var"##Ctag#302" +struct var"##Ctag#347" data::NTuple{16,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#302"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#347"}, f::Symbol) f === :uuidDev && return Ptr{CUuuid}(x + 0) - f === :npu && return Ptr{var"##Ctag#303"}(x + 0) + f === :npu && return Ptr{var"##Ctag#348"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#302", f::Symbol) - r = Ref{var"##Ctag#302"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#302"}, r) +function Base.getproperty(x::var"##Ctag#347", f::Symbol) + r = Ref{var"##Ctag#347"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#347"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#302"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#347"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#302", private::Bool=false) +function Base.propertynames(x::var"##Ctag#347", private::Bool=false) return (:uuidDev, :npu, if private fieldnames(typeof(x)) else @@ -6615,28 +6615,28 @@ function Base.propertynames(x::var"##Ctag#302", private::Bool=false) end...) end -struct var"##Ctag#304" +struct var"##Ctag#349" data::NTuple{16,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#304"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#349"}, f::Symbol) f === :uuidDev && return Ptr{CUuuid}(x + 0) - f === :npu && return Ptr{var"##Ctag#305"}(x + 0) + f === :npu && return Ptr{var"##Ctag#350"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#304", f::Symbol) - r = Ref{var"##Ctag#304"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#304"}, r) +function Base.getproperty(x::var"##Ctag#349", f::Symbol) + r = Ref{var"##Ctag#349"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#349"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#304"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#349"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#304", private::Bool=false) +function Base.propertynames(x::var"##Ctag#349", private::Bool=false) return (:uuidDev, :npu, if private fieldnames(typeof(x)) else @@ -6653,8 +6653,8 @@ function Base.getproperty(x::Ptr{CUpti_ActivityNvLink2}, f::Symbol) f === :nvlinkVersion && return Ptr{UInt32}(x + 4) f === :typeDev0 && return Ptr{CUpti_DevType}(x + 8) f === :typeDev1 && return Ptr{CUpti_DevType}(x + 12) - f === :idDev0 && return Ptr{var"##Ctag#302"}(x + 16) - f === :idDev1 && return Ptr{var"##Ctag#304"}(x + 32) + f === :idDev0 && return Ptr{var"##Ctag#347"}(x + 16) + f === :idDev1 && return Ptr{var"##Ctag#349"}(x + 32) f === :flag && return Ptr{UInt32}(x + 48) f === :physicalNvLinkCount && return Ptr{UInt32}(x + 52) f === :portDev0 && return Ptr{NTuple{32,Int8}}(x + 56) @@ -6684,28 +6684,28 @@ function Base.propertynames(x::CUpti_ActivityNvLink2, private::Bool=false) end...) end -struct var"##Ctag#296" +struct var"##Ctag#341" data::NTuple{16,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#296"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#341"}, f::Symbol) f === :uuidDev && return Ptr{CUuuid}(x + 0) - f === :npu && return Ptr{var"##Ctag#297"}(x + 0) + f === :npu && return Ptr{var"##Ctag#342"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#296", f::Symbol) - r = Ref{var"##Ctag#296"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#296"}, r) +function Base.getproperty(x::var"##Ctag#341", f::Symbol) + r = Ref{var"##Ctag#341"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#341"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#296"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#341"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#296", private::Bool=false) +function Base.propertynames(x::var"##Ctag#341", private::Bool=false) return (:uuidDev, :npu, if private fieldnames(typeof(x)) else @@ -6713,28 +6713,28 @@ function Base.propertynames(x::var"##Ctag#296", private::Bool=false) end...) end -struct var"##Ctag#298" +struct var"##Ctag#343" data::NTuple{16,UInt8} end -function Base.getproperty(x::Ptr{var"##Ctag#298"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#343"}, f::Symbol) f === :uuidDev && return Ptr{CUuuid}(x + 0) - f === :npu && return Ptr{var"##Ctag#299"}(x + 0) + f === :npu && return Ptr{var"##Ctag#344"}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#298", f::Symbol) - r = Ref{var"##Ctag#298"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#298"}, r) +function Base.getproperty(x::var"##Ctag#343", f::Symbol) + r = Ref{var"##Ctag#343"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#343"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#298"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#343"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -function Base.propertynames(x::var"##Ctag#298", private::Bool=false) +function Base.propertynames(x::var"##Ctag#343", private::Bool=false) return (:uuidDev, :npu, if private fieldnames(typeof(x)) else @@ -6751,8 +6751,8 @@ function Base.getproperty(x::Ptr{CUpti_ActivityNvLink3}, f::Symbol) f === :nvlinkVersion && return Ptr{UInt32}(x + 4) f === :typeDev0 && return Ptr{CUpti_DevType}(x + 8) f === :typeDev1 && return Ptr{CUpti_DevType}(x + 12) - f === :idDev0 && return Ptr{var"##Ctag#296"}(x + 16) - f === :idDev1 && return Ptr{var"##Ctag#298"}(x + 32) + f === :idDev0 && return Ptr{var"##Ctag#341"}(x + 16) + f === :idDev1 && return Ptr{var"##Ctag#343"}(x + 32) f === :flag && return Ptr{UInt32}(x + 48) f === :physicalNvLinkCount && return Ptr{UInt32}(x + 52) f === :portDev0 && return Ptr{NTuple{32,Int8}}(x + 56) @@ -8765,350 +8765,350 @@ end @gcsafe_ccall libcupti.cuptiProfilerDeviceSupported(pParams::Ptr{CUpti_Profiler_DeviceSupported_Params})::CUptiResult end -struct var"##Ctag#276" +struct var"##Ctag#321" index::UInt32 domainId::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#276"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#321"}, f::Symbol) f === :index && return Ptr{UInt32}(x + 0) f === :domainId && return Ptr{UInt32}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#276", f::Symbol) - r = Ref{var"##Ctag#276"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#276"}, r) +function Base.getproperty(x::var"##Ctag#321", f::Symbol) + r = Ref{var"##Ctag#321"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#321"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#276"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#321"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#278" +struct var"##Ctag#323" index::UInt32 domainId::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#278"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#323"}, f::Symbol) f === :index && return Ptr{UInt32}(x + 0) f === :domainId && return Ptr{UInt32}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#278", f::Symbol) - r = Ref{var"##Ctag#278"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#278"}, r) +function Base.getproperty(x::var"##Ctag#323", f::Symbol) + r = Ref{var"##Ctag#323"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#323"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#278"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#323"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#288" +struct var"##Ctag#333" requested::UInt8 executed::UInt8 end -function Base.getproperty(x::Ptr{var"##Ctag#288"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#333"}, f::Symbol) f === :requested && return (Ptr{UInt8}(x + 0), 0, 4) f === :executed && return (Ptr{UInt8}(x + 0), 4, 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#288", f::Symbol) - r = Ref{var"##Ctag#288"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#288"}, r) +function Base.getproperty(x::var"##Ctag#333", f::Symbol) + r = Ref{var"##Ctag#333"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#333"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#288"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#333"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#292" +struct var"##Ctag#337" requested::UInt8 executed::UInt8 end -function Base.getproperty(x::Ptr{var"##Ctag#292"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#337"}, f::Symbol) f === :requested && return (Ptr{UInt8}(x + 0), 0, 4) f === :executed && return (Ptr{UInt8}(x + 0), 4, 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#292", f::Symbol) - r = Ref{var"##Ctag#292"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#292"}, r) +function Base.getproperty(x::var"##Ctag#337", f::Symbol) + r = Ref{var"##Ctag#337"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#337"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#292"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#337"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#295" +struct var"##Ctag#340" requested::UInt8 executed::UInt8 end -function Base.getproperty(x::Ptr{var"##Ctag#295"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#340"}, f::Symbol) f === :requested && return (Ptr{UInt8}(x + 0), 0, 4) f === :executed && return (Ptr{UInt8}(x + 0), 4, 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#295", f::Symbol) - r = Ref{var"##Ctag#295"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#295"}, r) +function Base.getproperty(x::var"##Ctag#340", f::Symbol) + r = Ref{var"##Ctag#340"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#340"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#295"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#340"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#297" +struct var"##Ctag#342" index::UInt32 domainId::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#297"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#342"}, f::Symbol) f === :index && return Ptr{UInt32}(x + 0) f === :domainId && return Ptr{UInt32}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#297", f::Symbol) - r = Ref{var"##Ctag#297"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#297"}, r) +function Base.getproperty(x::var"##Ctag#342", f::Symbol) + r = Ref{var"##Ctag#342"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#342"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#297"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#342"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#299" +struct var"##Ctag#344" index::UInt32 domainId::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#299"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#344"}, f::Symbol) f === :index && return Ptr{UInt32}(x + 0) f === :domainId && return Ptr{UInt32}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#299", f::Symbol) - r = Ref{var"##Ctag#299"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#299"}, r) +function Base.getproperty(x::var"##Ctag#344", f::Symbol) + r = Ref{var"##Ctag#344"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#344"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#299"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#344"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#303" +struct var"##Ctag#348" index::UInt32 domainId::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#303"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#348"}, f::Symbol) f === :index && return Ptr{UInt32}(x + 0) f === :domainId && return Ptr{UInt32}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#303", f::Symbol) - r = Ref{var"##Ctag#303"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#303"}, r) +function Base.getproperty(x::var"##Ctag#348", f::Symbol) + r = Ref{var"##Ctag#348"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#348"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#303"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#348"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#305" +struct var"##Ctag#350" index::UInt32 domainId::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#305"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#350"}, f::Symbol) f === :index && return Ptr{UInt32}(x + 0) f === :domainId && return Ptr{UInt32}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#305", f::Symbol) - r = Ref{var"##Ctag#305"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#305"}, r) +function Base.getproperty(x::var"##Ctag#350", f::Symbol) + r = Ref{var"##Ctag#350"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#350"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#305"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#350"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#307" +struct var"##Ctag#352" requested::UInt8 executed::UInt8 end -function Base.getproperty(x::Ptr{var"##Ctag#307"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#352"}, f::Symbol) f === :requested && return (Ptr{UInt8}(x + 0), 0, 4) f === :executed && return (Ptr{UInt8}(x + 0), 4, 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#307", f::Symbol) - r = Ref{var"##Ctag#307"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#307"}, r) +function Base.getproperty(x::var"##Ctag#352", f::Symbol) + r = Ref{var"##Ctag#352"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#352"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#307"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#352"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#311" +struct var"##Ctag#356" requested::UInt8 executed::UInt8 end -function Base.getproperty(x::Ptr{var"##Ctag#311"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#356"}, f::Symbol) f === :requested && return (Ptr{UInt8}(x + 0), 0, 4) f === :executed && return (Ptr{UInt8}(x + 0), 4, 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#311", f::Symbol) - r = Ref{var"##Ctag#311"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#311"}, r) +function Base.getproperty(x::var"##Ctag#356", f::Symbol) + r = Ref{var"##Ctag#356"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#356"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#311"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#356"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#345" +struct var"##Ctag#390" requested::UInt8 executed::UInt8 end -function Base.getproperty(x::Ptr{var"##Ctag#345"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#390"}, f::Symbol) f === :requested && return (Ptr{UInt8}(x + 0), 0, 4) f === :executed && return (Ptr{UInt8}(x + 0), 4, 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#345", f::Symbol) - r = Ref{var"##Ctag#345"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#345"}, r) +function Base.getproperty(x::var"##Ctag#390", f::Symbol) + r = Ref{var"##Ctag#390"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#390"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#345"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#390"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#347" +struct var"##Ctag#392" requested::UInt8 executed::UInt8 end -function Base.getproperty(x::Ptr{var"##Ctag#347"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#392"}, f::Symbol) f === :requested && return (Ptr{UInt8}(x + 0), 0, 4) f === :executed && return (Ptr{UInt8}(x + 0), 4, 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#347", f::Symbol) - r = Ref{var"##Ctag#347"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#347"}, r) +function Base.getproperty(x::var"##Ctag#392", f::Symbol) + r = Ref{var"##Ctag#392"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#392"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#347"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#392"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#349" +struct var"##Ctag#394" index::UInt32 domainId::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#349"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#394"}, f::Symbol) f === :index && return Ptr{UInt32}(x + 0) f === :domainId && return Ptr{UInt32}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#349", f::Symbol) - r = Ref{var"##Ctag#349"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#349"}, r) +function Base.getproperty(x::var"##Ctag#394", f::Symbol) + r = Ref{var"##Ctag#394"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#394"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#349"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#394"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#351" +struct var"##Ctag#396" index::UInt32 domainId::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#351"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#396"}, f::Symbol) f === :index && return Ptr{UInt32}(x + 0) f === :domainId && return Ptr{UInt32}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#351", f::Symbol) - r = Ref{var"##Ctag#351"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#351"}, r) +function Base.getproperty(x::var"##Ctag#396", f::Symbol) + r = Ref{var"##Ctag#396"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#396"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#351"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#396"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#354" +struct var"##Ctag#399" requested::UInt8 executed::UInt8 end -function Base.getproperty(x::Ptr{var"##Ctag#354"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#399"}, f::Symbol) f === :requested && return (Ptr{UInt8}(x + 0), 0, 4) f === :executed && return (Ptr{UInt8}(x + 0), 4, 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#354", f::Symbol) - r = Ref{var"##Ctag#354"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#354"}, r) +function Base.getproperty(x::var"##Ctag#399", f::Symbol) + r = Ref{var"##Ctag#399"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#399"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#354"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#399"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#356" +struct var"##Ctag#401" smClock::UInt32 memoryClock::UInt32 pcieLinkGen::UInt32 pcieLinkWidth::UInt32 clocksThrottleReasons::CUpti_EnvironmentClocksThrottleReason end -function Base.getproperty(x::Ptr{var"##Ctag#356"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#401"}, f::Symbol) f === :smClock && return Ptr{UInt32}(x + 0) f === :memoryClock && return Ptr{UInt32}(x + 4) f === :pcieLinkGen && return Ptr{UInt32}(x + 8) @@ -9118,104 +9118,104 @@ function Base.getproperty(x::Ptr{var"##Ctag#356"}, f::Symbol) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#356", f::Symbol) - r = Ref{var"##Ctag#356"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#356"}, r) +function Base.getproperty(x::var"##Ctag#401", f::Symbol) + r = Ref{var"##Ctag#401"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#401"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#356"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#401"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#357" +struct var"##Ctag#402" gpuTemperature::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#357"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#402"}, f::Symbol) f === :gpuTemperature && return Ptr{UInt32}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#357", f::Symbol) - r = Ref{var"##Ctag#357"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#357"}, r) +function Base.getproperty(x::var"##Ctag#402", f::Symbol) + r = Ref{var"##Ctag#402"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#402"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#357"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#402"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#358" +struct var"##Ctag#403" power::UInt32 powerLimit::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#358"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#403"}, f::Symbol) f === :power && return Ptr{UInt32}(x + 0) f === :powerLimit && return Ptr{UInt32}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#358", f::Symbol) - r = Ref{var"##Ctag#358"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#358"}, r) +function Base.getproperty(x::var"##Ctag#403", f::Symbol) + r = Ref{var"##Ctag#403"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#403"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#358"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#403"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#359" +struct var"##Ctag#404" fanSpeed::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#359"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#404"}, f::Symbol) f === :fanSpeed && return Ptr{UInt32}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#359", f::Symbol) - r = Ref{var"##Ctag#359"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#359"}, r) +function Base.getproperty(x::var"##Ctag#404", f::Symbol) + r = Ref{var"##Ctag#404"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#404"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#359"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#404"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#362" +struct var"##Ctag#407" uuidDev::CUuuid peerDev::NTuple{32,CUdevice} end -function Base.getproperty(x::Ptr{var"##Ctag#362"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#407"}, f::Symbol) f === :uuidDev && return Ptr{CUuuid}(x + 0) f === :peerDev && return Ptr{NTuple{32,CUdevice}}(x + 16) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#362", f::Symbol) - r = Ref{var"##Ctag#362"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#362"}, r) +function Base.getproperty(x::var"##Ctag#407", f::Symbol) + r = Ref{var"##Ctag#407"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#407"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#362"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#407"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#363" +struct var"##Ctag#408" secondaryBus::UInt16 deviceId::UInt16 vendorId::UInt16 pad0::UInt16 end -function Base.getproperty(x::Ptr{var"##Ctag#363"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#408"}, f::Symbol) f === :secondaryBus && return Ptr{UInt16}(x + 0) f === :deviceId && return Ptr{UInt16}(x + 2) f === :vendorId && return Ptr{UInt16}(x + 4) @@ -9223,100 +9223,100 @@ function Base.getproperty(x::Ptr{var"##Ctag#363"}, f::Symbol) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#363", f::Symbol) - r = Ref{var"##Ctag#363"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#363"}, r) +function Base.getproperty(x::var"##Ctag#408", f::Symbol) + r = Ref{var"##Ctag#408"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#408"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#363"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#408"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#365" +struct var"##Ctag#410" requested::UInt8 executed::UInt8 end -function Base.getproperty(x::Ptr{var"##Ctag#365"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#410"}, f::Symbol) f === :requested && return (Ptr{UInt8}(x + 0), 0, 4) f === :executed && return (Ptr{UInt8}(x + 0), 4, 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#365", f::Symbol) - r = Ref{var"##Ctag#365"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#365"}, r) +function Base.getproperty(x::var"##Ctag#410", f::Symbol) + r = Ref{var"##Ctag#410"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#410"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#365"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#410"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#379" +struct var"##Ctag#424" requested::UInt8 executed::UInt8 end -function Base.getproperty(x::Ptr{var"##Ctag#379"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#424"}, f::Symbol) f === :requested && return (Ptr{UInt8}(x + 0), 0, 4) f === :executed && return (Ptr{UInt8}(x + 0), 4, 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#379", f::Symbol) - r = Ref{var"##Ctag#379"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#379"}, r) +function Base.getproperty(x::var"##Ctag#424", f::Symbol) + r = Ref{var"##Ctag#424"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#424"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#379"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#424"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#396" +struct var"##Ctag#441" processId::UInt32 threadId::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#396"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#441"}, f::Symbol) f === :processId && return Ptr{UInt32}(x + 0) f === :threadId && return Ptr{UInt32}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#396", f::Symbol) - r = Ref{var"##Ctag#396"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#396"}, r) +function Base.getproperty(x::var"##Ctag#441", f::Symbol) + r = Ref{var"##Ctag#441"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#441"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#396"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#441"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#397" +struct var"##Ctag#442" deviceId::UInt32 contextId::UInt32 streamId::UInt32 end -function Base.getproperty(x::Ptr{var"##Ctag#397"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#442"}, f::Symbol) f === :deviceId && return Ptr{UInt32}(x + 0) f === :contextId && return Ptr{UInt32}(x + 4) f === :streamId && return Ptr{UInt32}(x + 8) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#397", f::Symbol) - r = Ref{var"##Ctag#397"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#397"}, r) +function Base.getproperty(x::var"##Ctag#442", f::Symbol) + r = Ref{var"##Ctag#442"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#442"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#397"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#442"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end diff --git a/lib/custatevec/src/libcustatevec.jl b/lib/custatevec/src/libcustatevec.jl index 4fdb73bebd..25c1c1637b 100644 --- a/lib/custatevec/src/libcustatevec.jl +++ b/lib/custatevec/src/libcustatevec.jl @@ -100,6 +100,7 @@ end @cenum custatevecCollapseOp_t::UInt32 begin CUSTATEVEC_COLLAPSE_NONE = 0 CUSTATEVEC_COLLAPSE_NORMALIZE_AND_ZERO = 1 + CUSTATEVEC_COLLAPSE_RESET = 2 end @cenum custatevecComputeType_t::UInt32 begin @@ -170,7 +171,7 @@ end value::Ptr{Int32})::custatevecStatus_t end -# no prototype is found for this function at custatevec.h:532:8, please use with caution +# no prototype is found for this function at custatevec.h:533:8, please use with caution function custatevecGetVersion() @gcsafe_ccall libcustatevec.custatevecGetVersion()::Csize_t end @@ -214,7 +215,7 @@ end @gcsafe_ccall libcustatevec.custatevecLoggerSetMask(mask::Int32)::custatevecStatus_t end -# no prototype is found for this function at custatevec.h:632:1, please use with caution +# no prototype is found for this function at custatevec.h:633:1, please use with caution @checked function custatevecLoggerForceDisable() @gcsafe_ccall libcustatevec.custatevecLoggerForceDisable()::custatevecStatus_t end diff --git a/lib/cutensor/src/libcutensor.jl b/lib/cutensor/src/libcutensor.jl index f71d2a2b70..3650c44329 100644 --- a/lib/cutensor/src/libcutensor.jl +++ b/lib/cutensor/src/libcutensor.jl @@ -26,36 +26,7 @@ end end end -@cenum cutensorDataType_t::UInt32 begin - CUTENSOR_R_16F = 2 - CUTENSOR_C_16F = 6 - CUTENSOR_R_16BF = 14 - CUTENSOR_C_16BF = 15 - CUTENSOR_R_32F = 0 - CUTENSOR_C_32F = 4 - CUTENSOR_R_64F = 1 - CUTENSOR_C_64F = 5 - CUTENSOR_R_4I = 16 - CUTENSOR_C_4I = 17 - CUTENSOR_R_4U = 18 - CUTENSOR_C_4U = 19 - CUTENSOR_R_8I = 3 - CUTENSOR_C_8I = 7 - CUTENSOR_R_8U = 8 - CUTENSOR_C_8U = 9 - CUTENSOR_R_16I = 20 - CUTENSOR_C_16I = 21 - CUTENSOR_R_16U = 22 - CUTENSOR_C_16U = 23 - CUTENSOR_R_32I = 10 - CUTENSOR_C_32I = 11 - CUTENSOR_R_32U = 12 - CUTENSOR_C_32U = 13 - CUTENSOR_R_64I = 24 - CUTENSOR_C_64I = 25 - CUTENSOR_R_64U = 26 - CUTENSOR_C_64U = 27 -end +const cutensorDataType_t = cudaDataType_t @cenum cutensorOperator_t::UInt32 begin CUTENSOR_OP_IDENTITY = 1 @@ -187,6 +158,10 @@ mutable struct cutensorTensorDescriptor end const cutensorTensorDescriptor_t = Ptr{cutensorTensorDescriptor} +mutable struct cutensorBlockSparseTensorDescriptor end + +const cutensorBlockSparseTensorDescriptor_t = Ptr{cutensorBlockSparseTensorDescriptor} + # typedef void ( * cutensorLoggerCallback_t ) ( int32_t logLevel , const char * functionName , const char * message ) const cutensorLoggerCallback_t = Ptr{Cvoid} @@ -239,7 +214,7 @@ end numModes::UInt32, extent::Ptr{Int64}, stride::Ptr{Int64}, - dataType::cutensorDataType_t, + dataType::cudaDataType_t, alignmentRequirement::UInt32)::cutensorStatus_t end @@ -513,16 +488,74 @@ end stream::cudaStream_t)::cutensorStatus_t end +@checked function cutensorCreateBlockSparseTensorDescriptor(handle, desc, numModes, + numNonZeroBlocks, + numSectionsPerMode, extent, + nonZeroCoordinates, stride, + dataType) + initialize_context() + @gcsafe_ccall libcutensor.cutensorCreateBlockSparseTensorDescriptor(handle::cutensorHandle_t, + desc::Ptr{cutensorBlockSparseTensorDescriptor_t}, + numModes::UInt32, + numNonZeroBlocks::UInt64, + numSectionsPerMode::Ptr{UInt32}, + extent::Ptr{Int64}, + nonZeroCoordinates::Ptr{Int32}, + stride::Ptr{Int64}, + dataType::cudaDataType_t)::cutensorStatus_t +end + +@checked function cutensorDestroyBlockSparseTensorDescriptor(desc) + initialize_context() + @gcsafe_ccall libcutensor.cutensorDestroyBlockSparseTensorDescriptor(desc::cutensorBlockSparseTensorDescriptor_t)::cutensorStatus_t +end + +@checked function cutensorCreateBlockSparseContraction(handle, desc, descA, modeA, opA, + descB, modeB, opB, descC, modeC, opC, + descD, modeD, descCompute) + initialize_context() + @gcsafe_ccall libcutensor.cutensorCreateBlockSparseContraction(handle::cutensorHandle_t, + desc::Ptr{cutensorOperationDescriptor_t}, + descA::cutensorBlockSparseTensorDescriptor_t, + modeA::Ptr{Int32}, + opA::cutensorOperator_t, + descB::cutensorBlockSparseTensorDescriptor_t, + modeB::Ptr{Int32}, + opB::cutensorOperator_t, + descC::cutensorBlockSparseTensorDescriptor_t, + modeC::Ptr{Int32}, + opC::cutensorOperator_t, + descD::cutensorBlockSparseTensorDescriptor_t, + modeD::Ptr{Int32}, + descCompute::cutensorComputeDescriptor_t)::cutensorStatus_t +end + +@checked function cutensorBlockSparseContract(handle, plan, alpha, A, B, beta, C, D, + workspace, workspaceSize, stream) + initialize_context() + @gcsafe_ccall libcutensor.cutensorBlockSparseContract(handle::cutensorHandle_t, + plan::cutensorPlan_t, + alpha::Ptr{Cvoid}, + A::Ptr{Ptr{Cvoid}}, + B::Ptr{Ptr{Cvoid}}, + beta::Ptr{Cvoid}, + C::Ptr{Ptr{Cvoid}}, + D::Ptr{Ptr{Cvoid}}, + workspace::Ptr{Cvoid}, + workspaceSize::UInt64, + stream::cudaStream_t)::cutensorStatus_t +end + function cutensorGetErrorString(error) @gcsafe_ccall libcutensor.cutensorGetErrorString(error::cutensorStatus_t)::Cstring end -# no prototype is found for this function at cutensor.h:1102:8, please use with caution +# no prototype is found for this function at cutensor.h:1401:8, please use with caution function cutensorGetVersion() @gcsafe_ccall libcutensor.cutensorGetVersion()::Csize_t end -# no prototype is found for this function at cutensor.h:1108:8, please use with caution +# no prototype is found for this function at cutensor.h:1407:8, please use with caution function cutensorGetCudartVersion() @gcsafe_ccall libcutensor.cutensorGetCudartVersion()::Csize_t end @@ -552,7 +585,7 @@ end @gcsafe_ccall libcutensor.cutensorLoggerSetMask(mask::Int32)::cutensorStatus_t end -# no prototype is found for this function at cutensor.h:1159:18, please use with caution +# no prototype is found for this function at cutensor.h:1458:18, please use with caution @checked function cutensorLoggerForceDisable() initialize_context() @gcsafe_ccall libcutensor.cutensorLoggerForceDisable()::cutensorStatus_t diff --git a/lib/cutensornet/src/libcutensornet.jl b/lib/cutensornet/src/libcutensornet.jl index 6c4d6ae5c5..f45b193d34 100644 --- a/lib/cutensornet/src/libcutensornet.jl +++ b/lib/cutensornet/src/libcutensornet.jl @@ -71,6 +71,7 @@ end CUTENSORNET_NETWORK_INPUT_TENSORS_CONJUGATED = 11 CUTENSORNET_NETWORK_INPUT_TENSORS_NUM_REQUIRE_GRAD = 20 CUTENSORNET_NETWORK_INPUT_TENSORS_REQUIRE_GRAD = 21 + CUTENSORNET_NETWORK_COMPUTE_TYPE = 30 end @cenum cutensornetGraphAlgo_t::UInt32 begin @@ -86,7 +87,6 @@ end @cenum cutensornetOptimizerCost_t::UInt32 begin CUTENSORNET_OPTIMIZER_COST_FLOPS = 0 CUTENSORNET_OPTIMIZER_COST_TIME = 1 - CUTENSORNET_OPTIMIZER_COST_TIME_TUNED = 2 end @cenum cutensornetSmartOption_t::UInt32 begin @@ -139,6 +139,11 @@ end CUTENSORNET_CONTRACTION_AUTOTUNE_INTERMEDIATE_MODES = 1 end +@cenum cutensornetNetworkAutotunePreferenceAttributes_t::UInt32 begin + CUTENSORNET_NETWORK_AUTOTUNE_MAX_ITERATIONS = 0 + CUTENSORNET_NETWORK_AUTOTUNE_INTERMEDIATE_MODES = 1 +end + const cutensornetNetworkDescriptor_t = Ptr{Cvoid} const cutensornetContractionPlan_t = Ptr{Cvoid} @@ -218,6 +223,8 @@ const cutensornetContractionOptimizerInfo_t = Ptr{Cvoid} const cutensornetContractionAutotunePreference_t = Ptr{Cvoid} +const cutensornetNetworkAutotunePreference_t = Ptr{Cvoid} + const cutensornetSliceGroup_t = Ptr{Cvoid} struct cutensornetTensorQualifiers_t @@ -334,6 +341,8 @@ end const cutensornetStateSampler_t = Ptr{Cvoid} +const cutensornetStateProjectionMPS_t = Ptr{Cvoid} + @cenum cutensornetSamplerAttributes_t::UInt32 begin CUTENSORNET_SAMPLER_OPT_NUM_HYPER_SAMPLES = 0 CUTENSORNET_SAMPLER_CONFIG_NUM_HYPER_SAMPLES = 1 @@ -385,6 +394,20 @@ const cutensornetLoggerCallbackData_t = Ptr{Cvoid} CUTENSORNET_STATE_MPS_GAUGE_SIMPLE = 1 end +struct cutensornetMPSEnvBounds_t + lowerBound::Int32 + upperBound::Int32 +end + +@cenum cutensornetStateProjectionMPSOrthoOption_t::UInt32 begin + CUTENSORNET_STATE_PROJECTION_MPS_ORTHO_AUTO = 0 +end + +@cenum cutensornetStateProjectionMPSAttributes_t::UInt32 begin + CUTENSORNET_STATE_PROJECTION_MPS_CONFIG_ORTHO_OPTION = 0 + CUTENSORNET_STATE_PROJECTION_MPS_CONFIG_NUM_HYPER_SAMPLES = 10 +end + @checked function cutensornetCreate(handle) initialize_context() @gcsafe_ccall libcutensornet.cutensornetCreate(handle::Ptr{cutensornetHandle_t})::cutensornetStatus_t @@ -399,7 +422,7 @@ end extentsIn, stridesIn, modesIn, qualifiersIn, numModesOut, extentsOut, stridesOut, modesOut, dataType, - computeType, descNet) + computeType, networkDesc) initialize_context() @gcsafe_ccall libcutensornet.cutensornetCreateNetworkDescriptor(handle::cutensornetHandle_t, numInputs::Int32, @@ -414,39 +437,73 @@ end modesOut::Ptr{Int32}, dataType::cudaDataType_t, computeType::cutensornetComputeType_t, - descNet::Ptr{cutensornetNetworkDescriptor_t})::cutensornetStatus_t + networkDesc::Ptr{cutensornetNetworkDescriptor_t})::cutensornetStatus_t +end + +@checked function cutensornetCreateNetwork(handle, networkDesc) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetCreateNetwork(handle::cutensornetHandle_t, + networkDesc::Ptr{cutensornetNetworkDescriptor_t})::cutensornetStatus_t +end + +@checked function cutensornetDestroyNetworkDescriptor(networkDesc) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetDestroyNetworkDescriptor(networkDesc::cutensornetNetworkDescriptor_t)::cutensornetStatus_t +end + +@checked function cutensornetDestroyNetwork(networkDesc) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetDestroyNetwork(networkDesc::cutensornetNetworkDescriptor_t)::cutensornetStatus_t end -@checked function cutensornetDestroyNetworkDescriptor(desc) +@checked function cutensornetNetworkAppendTensor(handle, networkDesc, numModes, extents, + modeLabels, qualifiers, dataType, tensorId) initialize_context() - @gcsafe_ccall libcutensornet.cutensornetDestroyNetworkDescriptor(desc::cutensornetNetworkDescriptor_t)::cutensornetStatus_t + @gcsafe_ccall libcutensornet.cutensornetNetworkAppendTensor(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + numModes::Int32, + extents::Ptr{Int64}, + modeLabels::Ptr{Int32}, + qualifiers::Ptr{cutensornetTensorQualifiers_t}, + dataType::cudaDataType_t, + tensorId::Ptr{Int64})::cutensornetStatus_t end -@checked function cutensornetNetworkGetAttribute(handle, networkDesc, attr, buf, +@checked function cutensornetNetworkSetOutputTensor(handle, networkDesc, numModes, + modeLabels, dataType) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkSetOutputTensor(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + numModes::Int32, + modeLabels::Ptr{Int32}, + dataType::cudaDataType_t)::cutensornetStatus_t +end + +@checked function cutensornetNetworkGetAttribute(handle, networkDesc, attr, buffer, sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetNetworkGetAttribute(handle::cutensornetHandle_t, networkDesc::cutensornetNetworkDescriptor_t, attr::cutensornetNetworkAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end -@checked function cutensornetNetworkSetAttribute(handle, networkDesc, attr, buf, +@checked function cutensornetNetworkSetAttribute(handle, networkDesc, attr, buffer, sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetNetworkSetAttribute(handle::cutensornetHandle_t, networkDesc::cutensornetNetworkDescriptor_t, attr::cutensornetNetworkAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end -@checked function cutensornetGetOutputTensorDetails(handle, descNet, numModes, dataSize, +@checked function cutensornetGetOutputTensorDetails(handle, networkDesc, numModes, dataSize, modeLabels, extents, strides) initialize_context() @gcsafe_ccall libcutensornet.cutensornetGetOutputTensorDetails(handle::cutensornetHandle_t, - descNet::cutensornetNetworkDescriptor_t, + networkDesc::cutensornetNetworkDescriptor_t, numModes::Ptr{Int32}, dataSize::Ptr{Csize_t}, modeLabels::Ptr{Int32}, @@ -454,10 +511,11 @@ end strides::Ptr{Int64})::cutensornetStatus_t end -@checked function cutensornetGetOutputTensorDescriptor(handle, descNet, outputTensorDesc) +@checked function cutensornetGetOutputTensorDescriptor(handle, networkDesc, + outputTensorDesc) initialize_context() @gcsafe_ccall libcutensornet.cutensornetGetOutputTensorDescriptor(handle::cutensornetHandle_t, - descNet::cutensornetNetworkDescriptor_t, + networkDesc::cutensornetNetworkDescriptor_t, outputTensorDesc::Ptr{cutensornetTensorDescriptor_t})::cutensornetStatus_t end @@ -479,19 +537,20 @@ end workDesc::Ptr{cutensornetWorkspaceDescriptor_t})::cutensornetStatus_t end -@checked function cutensornetWorkspaceComputeSizes(handle, descNet, optimizerInfo, workDesc) +@checked function cutensornetWorkspaceComputeSizes(handle, networkDesc, optimizerInfo, + workDesc) initialize_context() @gcsafe_ccall libcutensornet.cutensornetWorkspaceComputeSizes(handle::cutensornetHandle_t, - descNet::cutensornetNetworkDescriptor_t, + networkDesc::cutensornetNetworkDescriptor_t, optimizerInfo::cutensornetContractionOptimizerInfo_t, workDesc::cutensornetWorkspaceDescriptor_t)::cutensornetStatus_t end -@checked function cutensornetWorkspaceComputeContractionSizes(handle, descNet, +@checked function cutensornetWorkspaceComputeContractionSizes(handle, networkDesc, optimizerInfo, workDesc) initialize_context() @gcsafe_ccall libcutensornet.cutensornetWorkspaceComputeContractionSizes(handle::cutensornetHandle_t, - descNet::cutensornetNetworkDescriptor_t, + networkDesc::cutensornetNetworkDescriptor_t, optimizerInfo::cutensornetContractionOptimizerInfo_t, workDesc::cutensornetWorkspaceDescriptor_t)::cutensornetStatus_t end @@ -566,9 +625,9 @@ end memSpace::cutensornetMemspace_t)::cutensornetStatus_t end -@checked function cutensornetDestroyWorkspaceDescriptor(desc) +@checked function cutensornetDestroyWorkspaceDescriptor(workDesc) initialize_context() - @gcsafe_ccall libcutensornet.cutensornetDestroyWorkspaceDescriptor(desc::cutensornetWorkspaceDescriptor_t)::cutensornetStatus_t + @gcsafe_ccall libcutensornet.cutensornetDestroyWorkspaceDescriptor(workDesc::cutensornetWorkspaceDescriptor_t)::cutensornetStatus_t end @checked function cutensornetCreateContractionOptimizerConfig(handle, optimizerConfig) @@ -583,22 +642,24 @@ end end @checked function cutensornetContractionOptimizerConfigGetAttribute(handle, optimizerConfig, - attr, buf, sizeInBytes) + attr, buffer, + sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetContractionOptimizerConfigGetAttribute(handle::cutensornetHandle_t, optimizerConfig::cutensornetContractionOptimizerConfig_t, attr::cutensornetContractionOptimizerConfigAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end @checked function cutensornetContractionOptimizerConfigSetAttribute(handle, optimizerConfig, - attr, buf, sizeInBytes) + attr, buffer, + sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetContractionOptimizerConfigSetAttribute(handle::cutensornetHandle_t, optimizerConfig::cutensornetContractionOptimizerConfig_t, attr::cutensornetContractionOptimizerConfigAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end @@ -607,40 +668,48 @@ end @gcsafe_ccall libcutensornet.cutensornetDestroyContractionOptimizerInfo(optimizerInfo::cutensornetContractionOptimizerInfo_t)::cutensornetStatus_t end -@checked function cutensornetCreateContractionOptimizerInfo(handle, descNet, optimizerInfo) +@checked function cutensornetCreateContractionOptimizerInfo(handle, networkDesc, + optimizerInfo) initialize_context() @gcsafe_ccall libcutensornet.cutensornetCreateContractionOptimizerInfo(handle::cutensornetHandle_t, - descNet::cutensornetNetworkDescriptor_t, + networkDesc::cutensornetNetworkDescriptor_t, optimizerInfo::Ptr{cutensornetContractionOptimizerInfo_t})::cutensornetStatus_t end -@checked function cutensornetContractionOptimize(handle, descNet, optimizerConfig, +@checked function cutensornetContractionOptimize(handle, networkDesc, optimizerConfig, workspaceSizeConstraint, optimizerInfo) initialize_context() @gcsafe_ccall libcutensornet.cutensornetContractionOptimize(handle::cutensornetHandle_t, - descNet::cutensornetNetworkDescriptor_t, + networkDesc::cutensornetNetworkDescriptor_t, optimizerConfig::cutensornetContractionOptimizerConfig_t, workspaceSizeConstraint::UInt64, optimizerInfo::cutensornetContractionOptimizerInfo_t)::cutensornetStatus_t end +@checked function cutensornetNetworkSetOptimizerInfo(handle, networkDesc, optimizerInfo) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkSetOptimizerInfo(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + optimizerInfo::cutensornetContractionOptimizerInfo_t)::cutensornetStatus_t +end + @checked function cutensornetContractionOptimizerInfoGetAttribute(handle, optimizerInfo, - attr, buf, sizeInBytes) + attr, buffer, sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetContractionOptimizerInfoGetAttribute(handle::cutensornetHandle_t, optimizerInfo::cutensornetContractionOptimizerInfo_t, attr::cutensornetContractionOptimizerInfoAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end @checked function cutensornetContractionOptimizerInfoSetAttribute(handle, optimizerInfo, - attr, buf, sizeInBytes) + attr, buffer, sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetContractionOptimizerInfoSetAttribute(handle::cutensornetHandle_t, optimizerInfo::cutensornetContractionOptimizerInfo_t, attr::cutensornetContractionOptimizerInfoAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end @@ -661,13 +730,14 @@ end sizeInBytes::Csize_t)::cutensornetStatus_t end -@checked function cutensornetCreateContractionOptimizerInfoFromPackedData(handle, descNet, +@checked function cutensornetCreateContractionOptimizerInfoFromPackedData(handle, + networkDesc, buffer, sizeInBytes, optimizerInfo) initialize_context() @gcsafe_ccall libcutensornet.cutensornetCreateContractionOptimizerInfoFromPackedData(handle::cutensornetHandle_t, - descNet::cutensornetNetworkDescriptor_t, + networkDesc::cutensornetNetworkDescriptor_t, buffer::Ptr{Cvoid}, sizeInBytes::Csize_t, optimizerInfo::Ptr{cutensornetContractionOptimizerInfo_t})::cutensornetStatus_t @@ -683,16 +753,23 @@ end optimizerInfo::cutensornetContractionOptimizerInfo_t)::cutensornetStatus_t end -@checked function cutensornetCreateContractionPlan(handle, descNet, optimizerInfo, workDesc, - plan) +@checked function cutensornetCreateContractionPlan(handle, networkDesc, optimizerInfo, + workDesc, plan) initialize_context() @gcsafe_ccall libcutensornet.cutensornetCreateContractionPlan(handle::cutensornetHandle_t, - descNet::cutensornetNetworkDescriptor_t, + networkDesc::cutensornetNetworkDescriptor_t, optimizerInfo::cutensornetContractionOptimizerInfo_t, workDesc::cutensornetWorkspaceDescriptor_t, plan::Ptr{cutensornetContractionPlan_t})::cutensornetStatus_t end +@checked function cutensornetNetworkPrepareContraction(handle, networkDesc, workDesc) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkPrepareContraction(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + workDesc::cutensornetWorkspaceDescriptor_t)::cutensornetStatus_t +end + @checked function cutensornetDestroyContractionPlan(plan) initialize_context() @gcsafe_ccall libcutensornet.cutensornetDestroyContractionPlan(plan::cutensornetContractionPlan_t)::cutensornetStatus_t @@ -710,41 +787,84 @@ end stream::cudaStream_t)::cutensornetStatus_t end +@checked function cutensornetNetworkAutotuneContraction(handle, networkDesc, workDesc, pref, + stream) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkAutotuneContraction(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + workDesc::cutensornetWorkspaceDescriptor_t, + pref::cutensornetNetworkAutotunePreference_t, + stream::cudaStream_t)::cutensornetStatus_t +end + @checked function cutensornetCreateContractionAutotunePreference(handle, autotunePreference) initialize_context() @gcsafe_ccall libcutensornet.cutensornetCreateContractionAutotunePreference(handle::cutensornetHandle_t, autotunePreference::Ptr{cutensornetContractionAutotunePreference_t})::cutensornetStatus_t end +@checked function cutensornetCreateNetworkAutotunePreference(handle, autotunePreference) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetCreateNetworkAutotunePreference(handle::cutensornetHandle_t, + autotunePreference::Ptr{cutensornetNetworkAutotunePreference_t})::cutensornetStatus_t +end + @checked function cutensornetContractionAutotunePreferenceGetAttribute(handle, autotunePreference, - attr, buf, + attr, buffer, sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetContractionAutotunePreferenceGetAttribute(handle::cutensornetHandle_t, autotunePreference::cutensornetContractionAutotunePreference_t, attr::cutensornetContractionAutotunePreferenceAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end +@checked function cutensornetNetworkAutotunePreferenceGetAttribute(handle, + autotunePreference, attr, + buffer, sizeInBytes) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkAutotunePreferenceGetAttribute(handle::cutensornetHandle_t, + autotunePreference::cutensornetNetworkAutotunePreference_t, + attr::cutensornetNetworkAutotunePreferenceAttributes_t, + buffer::Ptr{Cvoid}, + sizeInBytes::Csize_t)::cutensornetStatus_t +end + @checked function cutensornetContractionAutotunePreferenceSetAttribute(handle, autotunePreference, - attr, buf, + attr, buffer, sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetContractionAutotunePreferenceSetAttribute(handle::cutensornetHandle_t, autotunePreference::cutensornetContractionAutotunePreference_t, attr::cutensornetContractionAutotunePreferenceAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end +@checked function cutensornetNetworkAutotunePreferenceSetAttribute(handle, + autotunePreference, attr, + buf, sizeInBytes) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkAutotunePreferenceSetAttribute(handle::cutensornetHandle_t, + autotunePreference::cutensornetNetworkAutotunePreference_t, + attr::cutensornetNetworkAutotunePreferenceAttributes_t, + buf::Ptr{Cvoid}, + sizeInBytes::Csize_t)::cutensornetStatus_t +end + @checked function cutensornetDestroyContractionAutotunePreference(autotunePreference) initialize_context() @gcsafe_ccall libcutensornet.cutensornetDestroyContractionAutotunePreference(autotunePreference::cutensornetContractionAutotunePreference_t)::cutensornetStatus_t end +@checked function cutensornetDestroyNetworkAutotunePreference(autotunePreference) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetDestroyNetworkAutotunePreference(autotunePreference::cutensornetNetworkAutotunePreference_t)::cutensornetStatus_t +end + @checked function cutensornetContraction(handle, plan, rawDataIn, rawDataOut, workDesc, sliceId, stream) initialize_context() @@ -794,35 +914,90 @@ end stream::cudaStream_t)::cutensornetStatus_t end -@checked function cutensornetComputeGradientsBackward(handle, plan, rawDataIn, - outputGradient, gradients, - accumulateOutput, workDesc, stream) +@checked function cutensornetNetworkSetInputTensorMemory(handle, networkDesc, tensorId, + buffer, strides) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkSetInputTensorMemory(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + tensorId::Int64, + buffer::Ptr{Cvoid}, + strides::Ptr{Int64})::cutensornetStatus_t +end + +@checked function cutensornetNetworkSetOutputTensorMemory(handle, networkDesc, buffer, + strides) initialize_context() - @gcsafe_ccall libcutensornet.cutensornetComputeGradientsBackward(handle::cutensornetHandle_t, - plan::cutensornetContractionPlan_t, - rawDataIn::Ptr{Ptr{Cvoid}}, - outputGradient::Ptr{Cvoid}, - gradients::Ptr{Ptr{Cvoid}}, - accumulateOutput::Int32, - workDesc::cutensornetWorkspaceDescriptor_t, - stream::cudaStream_t)::cutensornetStatus_t + @gcsafe_ccall libcutensornet.cutensornetNetworkSetOutputTensorMemory(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + buffer::Ptr{Cvoid}, + strides::Ptr{Int64})::cutensornetStatus_t +end + +@checked function cutensornetNetworkSetGradientTensorMemory(handle, networkDesc, + correspondingTensorId, buffer, + strides) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkSetGradientTensorMemory(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + correspondingTensorId::Int64, + buffer::Ptr{Cvoid}, + strides::Ptr{Int64})::cutensornetStatus_t +end + +@checked function cutensornetNetworkSetAdjointTensorMemory(handle, networkDesc, buffer, + strides) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkSetAdjointTensorMemory(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + buffer::Ptr{Cvoid}, + strides::Ptr{Int64})::cutensornetStatus_t +end + +@checked function cutensornetNetworkContract(handle, networkDesc, accumulateOutput, + workDesc, sliceGroup, stream) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkContract(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + accumulateOutput::Int32, + workDesc::cutensornetWorkspaceDescriptor_t, + sliceGroup::cutensornetSliceGroup_t, + stream::cudaStream_t)::cutensornetStatus_t +end + +@checked function cutensornetNetworkPrepareGradientsBackward(handle, networkDesc, workDesc) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkPrepareGradientsBackward(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + workDesc::cutensornetWorkspaceDescriptor_t)::cutensornetStatus_t +end + +@checked function cutensornetNetworkComputeGradientsBackward(handle, networkDesc, + accumulateOutput, workDesc, + sliceGroup, stream) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetNetworkComputeGradientsBackward(handle::cutensornetHandle_t, + networkDesc::cutensornetNetworkDescriptor_t, + accumulateOutput::Int32, + workDesc::cutensornetWorkspaceDescriptor_t, + sliceGroup::cutensornetSliceGroup_t, + stream::cudaStream_t)::cutensornetStatus_t end @checked function cutensornetCreateTensorDescriptor(handle, numModes, extents, strides, - modes, dataType, descTensor) + modeLabels, dataType, tensorDesc) initialize_context() @gcsafe_ccall libcutensornet.cutensornetCreateTensorDescriptor(handle::cutensornetHandle_t, numModes::Int32, extents::Ptr{Int64}, strides::Ptr{Int64}, - modes::Ptr{Int32}, + modeLabels::Ptr{Int32}, dataType::cudaDataType_t, - descTensor::Ptr{cutensornetTensorDescriptor_t})::cutensornetStatus_t + tensorDesc::Ptr{cutensornetTensorDescriptor_t})::cutensornetStatus_t end -@checked function cutensornetDestroyTensorDescriptor(descTensor) +@checked function cutensornetDestroyTensorDescriptor(tensorDesc) initialize_context() - @gcsafe_ccall libcutensornet.cutensornetDestroyTensorDescriptor(descTensor::cutensornetTensorDescriptor_t)::cutensornetStatus_t + @gcsafe_ccall libcutensornet.cutensornetDestroyTensorDescriptor(tensorDesc::cutensornetTensorDescriptor_t)::cutensornetStatus_t end @checked function cutensornetCreateTensorSVDConfig(handle, svdConfig) @@ -836,23 +1011,23 @@ end @gcsafe_ccall libcutensornet.cutensornetDestroyTensorSVDConfig(svdConfig::cutensornetTensorSVDConfig_t)::cutensornetStatus_t end -@checked function cutensornetTensorSVDConfigGetAttribute(handle, svdConfig, attr, buf, +@checked function cutensornetTensorSVDConfigGetAttribute(handle, svdConfig, attr, buffer, sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetTensorSVDConfigGetAttribute(handle::cutensornetHandle_t, svdConfig::cutensornetTensorSVDConfig_t, attr::cutensornetTensorSVDConfigAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end -@checked function cutensornetTensorSVDConfigSetAttribute(handle, svdConfig, attr, buf, +@checked function cutensornetTensorSVDConfigSetAttribute(handle, svdConfig, attr, buffer, sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetTensorSVDConfigSetAttribute(handle::cutensornetHandle_t, svdConfig::cutensornetTensorSVDConfig_t, attr::cutensornetTensorSVDConfigAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end @@ -883,13 +1058,13 @@ end svdInfo::Ptr{cutensornetTensorSVDInfo_t})::cutensornetStatus_t end -@checked function cutensornetTensorSVDInfoGetAttribute(handle, svdInfo, attr, buf, +@checked function cutensornetTensorSVDInfoGetAttribute(handle, svdInfo, attr, buffer, sizeInBytes) initialize_context() @gcsafe_ccall libcutensornet.cutensornetTensorSVDInfoGetAttribute(handle::cutensornetHandle_t, svdInfo::cutensornetTensorSVDInfo_t, attr::cutensornetTensorSVDInfoAttributes_t, - buf::Ptr{Cvoid}, + buffer::Ptr{Cvoid}, sizeInBytes::Csize_t)::cutensornetStatus_t end @@ -1009,17 +1184,17 @@ end @gcsafe_ccall libcutensornet.cutensornetLoggerSetMask(mask::Int32)::cutensornetStatus_t end -# no prototype is found for this function at cutensornet.h:1269:21, please use with caution +# no prototype is found for this function at cutensornet.h:1586:21, please use with caution @checked function cutensornetLoggerForceDisable() @gcsafe_ccall libcutensornet.cutensornetLoggerForceDisable()::cutensornetStatus_t end -# no prototype is found for this function at cutensornet.h:1274:8, please use with caution +# no prototype is found for this function at cutensornet.h:1591:8, please use with caution function cutensornetGetVersion() @gcsafe_ccall libcutensornet.cutensornetGetVersion()::Csize_t end -# no prototype is found for this function at cutensornet.h:1280:8, please use with caution +# no prototype is found for this function at cutensornet.h:1597:8, please use with caution function cutensornetGetCudartVersion() @gcsafe_ccall libcutensornet.cutensornetGetCudartVersion()::Csize_t end @@ -1557,4 +1732,120 @@ end @gcsafe_ccall libcutensornet.cutensornetDestroySampler(tensorNetworkSampler::cutensornetStateSampler_t)::cutensornetStatus_t end +@checked function cutensornetCreateStateProjectionMPS(handle, numStates, + tensorNetworkStates, coeffs, + symmetric, numEnvs, specEnvs, + boundaryCondition, numTensors, + quditsPerTensor, extentsOut, + stridesOut, dualTensorsDataOut, + orthoSpec, tensorNetworkProjection) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetCreateStateProjectionMPS(handle::cutensornetHandle_t, + numStates::Int32, + tensorNetworkStates::Ptr{cutensornetState_t}, + coeffs::Ptr{cuDoubleComplex}, + symmetric::Int32, + numEnvs::Int32, + specEnvs::Ptr{cutensornetMPSEnvBounds_t}, + boundaryCondition::cutensornetBoundaryCondition_t, + numTensors::Int32, + quditsPerTensor::Ptr{Int32}, + extentsOut::Ptr{Ptr{Int64}}, + stridesOut::Ptr{Ptr{Int64}}, + dualTensorsDataOut::Ptr{Ptr{Cvoid}}, + orthoSpec::Ptr{cutensornetMPSEnvBounds_t}, + tensorNetworkProjection::Ptr{cutensornetStateProjectionMPS_t})::cutensornetStatus_t +end + +@checked function cutensornetStateProjectionMPSConfigure(handle, tensorNetworkProjection, + attribute, attributeValue, + attributeSize) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetStateProjectionMPSConfigure(handle::cutensornetHandle_t, + tensorNetworkProjection::cutensornetStateProjectionMPS_t, + attribute::cutensornetStateProjectionMPSAttributes_t, + attributeValue::Ptr{Cvoid}, + attributeSize::Csize_t)::cutensornetStatus_t +end + +@checked function cutensornetStateProjectionMPSPrepare(handle, tensorNetworkProjection, + maxWorkspaceSizeDevice, workDesc, + cudaStream) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetStateProjectionMPSPrepare(handle::cutensornetHandle_t, + tensorNetworkProjection::cutensornetStateProjectionMPS_t, + maxWorkspaceSizeDevice::Csize_t, + workDesc::cutensornetWorkspaceDescriptor_t, + cudaStream::cudaStream_t)::cutensornetStatus_t +end + +@checked function cutensornetStateProjectionMPSComputeTensorEnv(handle, + tensorNetworkProjection, + envSpec, stridesIn, + envTensorDataIn, stridesOut, + envTensorDataOut, + applyInvMetric, + reResolveChannels, workDesc, + cudaStream) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetStateProjectionMPSComputeTensorEnv(handle::cutensornetHandle_t, + tensorNetworkProjection::cutensornetStateProjectionMPS_t, + envSpec::Ptr{cutensornetMPSEnvBounds_t}, + stridesIn::Ptr{Int64}, + envTensorDataIn::Ptr{Cvoid}, + stridesOut::Ptr{Int64}, + envTensorDataOut::Ptr{Cvoid}, + applyInvMetric::Int32, + reResolveChannels::Int32, + workDesc::cutensornetWorkspaceDescriptor_t, + cudaStream::cudaStream_t)::cutensornetStatus_t +end + +@checked function cutensornetStateProjectionMPSGetTensorInfo(handle, + tensorNetworkProjection, + envSpec, extents, + recommendedStrides) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetStateProjectionMPSGetTensorInfo(handle::cutensornetHandle_t, + tensorNetworkProjection::cutensornetStateProjectionMPS_t, + envSpec::Ptr{cutensornetMPSEnvBounds_t}, + extents::Ptr{Int64}, + recommendedStrides::Ptr{Int64})::cutensornetStatus_t +end + +@checked function cutensornetStateProjectionMPSExtractTensor(handle, + tensorNetworkProjection, + envSpec, strides, + envTensorData, workDesc, + cudaStream) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetStateProjectionMPSExtractTensor(handle::cutensornetHandle_t, + tensorNetworkProjection::cutensornetStateProjectionMPS_t, + envSpec::Ptr{cutensornetMPSEnvBounds_t}, + strides::Ptr{Int64}, + envTensorData::Ptr{Cvoid}, + workDesc::cutensornetWorkspaceDescriptor_t, + cudaStream::cudaStream_t)::cutensornetStatus_t +end + +@checked function cutensornetStateProjectionMPSInsertTensor(handle, tensorNetworkProjection, + envSpec, orthoSpec, strides, + envTensorData, workDesc, + cudaStream) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetStateProjectionMPSInsertTensor(handle::cutensornetHandle_t, + tensorNetworkProjection::cutensornetStateProjectionMPS_t, + envSpec::Ptr{cutensornetMPSEnvBounds_t}, + orthoSpec::Ptr{cutensornetMPSEnvBounds_t}, + strides::Ptr{Int64}, + envTensorData::Ptr{Cvoid}, + workDesc::cutensornetWorkspaceDescriptor_t, + cudaStream::cudaStream_t)::cutensornetStatus_t +end + +@checked function cutensornetDestroyStateProjectionMPS(tensorNetworkProjection) + initialize_context() + @gcsafe_ccall libcutensornet.cutensornetDestroyStateProjectionMPS(tensorNetworkProjection::cutensornetStateProjectionMPS_t)::cutensornetStatus_t +end + const CUTENSORNET_ALLOCATOR_NAME_LEN = 64 diff --git a/lib/nvml/libnvml.jl b/lib/nvml/libnvml.jl index 525a34dab6..704041694c 100644 --- a/lib/nvml/libnvml.jl +++ b/lib/nvml/libnvml.jl @@ -488,14 +488,14 @@ end NVML_THERMAL_CONTROLLER_UNKNOWN = -1 end -struct var"##Ctag#272" +struct var"##Ctag#317" controller::nvmlThermalController_t defaultMinTemp::Cint defaultMaxTemp::Cint currentTemp::Cint target::nvmlThermalTarget_t end -function Base.getproperty(x::Ptr{var"##Ctag#272"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#317"}, f::Symbol) f === :controller && return Ptr{nvmlThermalController_t}(x + 0) f === :defaultMinTemp && return Ptr{Cint}(x + 4) f === :defaultMaxTemp && return Ptr{Cint}(x + 8) @@ -504,14 +504,14 @@ function Base.getproperty(x::Ptr{var"##Ctag#272"}, f::Symbol) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#272", f::Symbol) - r = Ref{var"##Ctag#272"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#272"}, r) +function Base.getproperty(x::var"##Ctag#317", f::Symbol) + r = Ref{var"##Ctag#317"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#317"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#272"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#317"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end @@ -521,7 +521,7 @@ end function Base.getproperty(x::Ptr{nvmlGpuThermalSettings_t}, f::Symbol) f === :count && return Ptr{Cuint}(x + 0) - f === :sensor && return Ptr{NTuple{3,var"##Ctag#272"}}(x + 4) + f === :sensor && return Ptr{NTuple{3,var"##Ctag#317"}}(x + 4) return getfield(x, f) end @@ -1043,13 +1043,13 @@ const nvmlPowerSource_t = Cuint NVML_GPU_UTILIZATION_DOMAIN_BUS = 3 end -struct var"##Ctag#270" +struct var"##Ctag#315" bIsPresent::Cuint percentage::Cuint incThreshold::Cuint decThreshold::Cuint end -function Base.getproperty(x::Ptr{var"##Ctag#270"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#315"}, f::Symbol) f === :bIsPresent && return Ptr{Cuint}(x + 0) f === :percentage && return Ptr{Cuint}(x + 4) f === :incThreshold && return Ptr{Cuint}(x + 8) @@ -1057,14 +1057,14 @@ function Base.getproperty(x::Ptr{var"##Ctag#270"}, f::Symbol) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#270", f::Symbol) - r = Ref{var"##Ctag#270"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#270"}, r) +function Base.getproperty(x::var"##Ctag#315", f::Symbol) + r = Ref{var"##Ctag#315"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#315"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#270"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#315"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end @@ -1074,7 +1074,7 @@ end function Base.getproperty(x::Ptr{nvmlGpuDynamicPstatesInfo_st}, f::Symbol) f === :flags && return Ptr{Cuint}(x + 0) - f === :utilization && return Ptr{NTuple{8,var"##Ctag#270"}}(x + 4) + f === :utilization && return Ptr{NTuple{8,var"##Ctag#315"}}(x + 4) return getfield(x, f) end @@ -1355,8 +1355,8 @@ struct nvmlVgpuSchedulerParams_t end function Base.getproperty(x::Ptr{nvmlVgpuSchedulerParams_t}, f::Symbol) - f === :vgpuSchedDataWithARR && return Ptr{var"##Ctag#268"}(x + 0) - f === :vgpuSchedData && return Ptr{var"##Ctag#269"}(x + 0) + f === :vgpuSchedDataWithARR && return Ptr{var"##Ctag#313"}(x + 0) + f === :vgpuSchedData && return Ptr{var"##Ctag#314"}(x + 0) return getfield(x, f) end @@ -1463,8 +1463,8 @@ struct nvmlVgpuSchedulerSetParams_t end function Base.getproperty(x::Ptr{nvmlVgpuSchedulerSetParams_t}, f::Symbol) - f === :vgpuSchedDataWithARR && return Ptr{var"##Ctag#273"}(x + 0) - f === :vgpuSchedData && return Ptr{var"##Ctag#274"}(x + 0) + f === :vgpuSchedDataWithARR && return Ptr{var"##Ctag#318"}(x + 0) + f === :vgpuSchedData && return Ptr{var"##Ctag#319"}(x + 0) return getfield(x, f) end @@ -4892,26 +4892,26 @@ mutable struct nvmlGpmSample_st end const nvmlGpmSample_t = Ptr{nvmlGpmSample_st} -struct var"##Ctag#271" +struct var"##Ctag#316" shortName::Cstring longName::Cstring unit::Cstring end -function Base.getproperty(x::Ptr{var"##Ctag#271"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#316"}, f::Symbol) f === :shortName && return Ptr{Cstring}(x + 0) f === :longName && return Ptr{Cstring}(x + 8) f === :unit && return Ptr{Cstring}(x + 16) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#271", f::Symbol) - r = Ref{var"##Ctag#271"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#271"}, r) +function Base.getproperty(x::var"##Ctag#316", f::Symbol) + r = Ref{var"##Ctag#316"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#316"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#271"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#316"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end @@ -4923,7 +4923,7 @@ function Base.getproperty(x::Ptr{nvmlGpmMetric_t}, f::Symbol) f === :metricId && return Ptr{Cuint}(x + 0) f === :nvmlReturn && return Ptr{nvmlReturn_t}(x + 4) f === :value && return Ptr{Cdouble}(x + 8) - f === :metricInfo && return Ptr{var"##Ctag#271"}(x + 16) + f === :metricInfo && return Ptr{var"##Ctag#316"}(x + 16) return getfield(x, f) end @@ -5286,83 +5286,83 @@ end pending::Ptr{nvmlDriverModel_t})::nvmlReturn_t end -struct var"##Ctag#268" +struct var"##Ctag#313" avgFactor::Cuint timeslice::Cuint end -function Base.getproperty(x::Ptr{var"##Ctag#268"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#313"}, f::Symbol) f === :avgFactor && return Ptr{Cuint}(x + 0) f === :timeslice && return Ptr{Cuint}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#268", f::Symbol) - r = Ref{var"##Ctag#268"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#268"}, r) +function Base.getproperty(x::var"##Ctag#313", f::Symbol) + r = Ref{var"##Ctag#313"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#313"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#268"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#313"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#269" +struct var"##Ctag#314" timeslice::Cuint end -function Base.getproperty(x::Ptr{var"##Ctag#269"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#314"}, f::Symbol) f === :timeslice && return Ptr{Cuint}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#269", f::Symbol) - r = Ref{var"##Ctag#269"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#269"}, r) +function Base.getproperty(x::var"##Ctag#314", f::Symbol) + r = Ref{var"##Ctag#314"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#314"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#269"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#314"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#273" +struct var"##Ctag#318" avgFactor::Cuint frequency::Cuint end -function Base.getproperty(x::Ptr{var"##Ctag#273"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#318"}, f::Symbol) f === :avgFactor && return Ptr{Cuint}(x + 0) f === :frequency && return Ptr{Cuint}(x + 4) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#273", f::Symbol) - r = Ref{var"##Ctag#273"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#273"}, r) +function Base.getproperty(x::var"##Ctag#318", f::Symbol) + r = Ref{var"##Ctag#318"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#318"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#273"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#318"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end -struct var"##Ctag#274" +struct var"##Ctag#319" timeslice::Cuint end -function Base.getproperty(x::Ptr{var"##Ctag#274"}, f::Symbol) +function Base.getproperty(x::Ptr{var"##Ctag#319"}, f::Symbol) f === :timeslice && return Ptr{Cuint}(x + 0) return getfield(x, f) end -function Base.getproperty(x::var"##Ctag#274", f::Symbol) - r = Ref{var"##Ctag#274"}(x) - ptr = Base.unsafe_convert(Ptr{var"##Ctag#274"}, r) +function Base.getproperty(x::var"##Ctag#319", f::Symbol) + r = Ref{var"##Ctag#319"}(x) + ptr = Base.unsafe_convert(Ptr{var"##Ctag#319"}, r) fptr = getproperty(ptr, f) GC.@preserve r unsafe_load(fptr) end -function Base.setproperty!(x::Ptr{var"##Ctag#274"}, f::Symbol, v) +function Base.setproperty!(x::Ptr{var"##Ctag#319"}, f::Symbol, v) return unsafe_store!(getproperty(x, f), v) end diff --git a/res/wrap/Manifest.toml b/res/wrap/Manifest.toml index 56ec6159d9..b16ab50fae 100644 --- a/res/wrap/Manifest.toml +++ b/res/wrap/Manifest.toml @@ -1,8 +1,8 @@ # This file is machine-generated - editing it directly is not advised -julia_version = "1.11.7" +julia_version = "1.12.1" manifest_format = "2.0" -project_hash = "5b3c7158524d47009a2aa20dc74e938a8cbc2050" +project_hash = "5a83d62eeab8c5071d89af0280b4eadc267f7dbe" [[deps.ArgTools]] uuid = "0dad84c5-d112-42e6-8d28-ef12dabb789f" @@ -29,33 +29,33 @@ version = "3.4.3" [[deps.CUDA_Driver_jll]] deps = ["Artifacts", "JLLWrappers", "Libdl", "Pkg"] -git-tree-sha1 = "12621de83838b5ce6a185050db5a184f4540679b" +git-tree-sha1 = "2023be0b10c56d259ea84a94dbfc021aa452f2c6" uuid = "4ee394cb-3365-5eb0-8335-949819d2adfc" -version = "13.0.0+0" +version = "13.0.2+0" [[deps.CUDA_Runtime_jll]] deps = ["Artifacts", "CUDA_Driver_jll", "JLLWrappers", "LazyArtifacts", "Libdl", "TOML"] -git-tree-sha1 = "cc727d90c9769db27945219f9ba149dbddc74f06" +git-tree-sha1 = "92cd84e2b760e471d647153ea5efc5789fc5e8b2" uuid = "76a88914-d11a-5bdc-97e0-2f5a05c973a2" -version = "0.19.0+0" +version = "0.19.2+0" [[deps.CUDA_SDK_jll]] deps = ["Artifacts", "JLLWrappers", "Libdl"] -git-tree-sha1 = "5339fb33822050be94823965725915c1beada4f8" +git-tree-sha1 = "8c546633bdb21b7b806276c0677a5656b4f675bc" uuid = "6cbf2f2e-7e60-5632-ac76-dca2274e0be0" -version = "13.0.1+1" +version = "13.0.2+1" [[deps.CUDNN_jll]] deps = ["Artifacts", "CUDA_Runtime_jll", "JLLWrappers", "LazyArtifacts", "Libdl", "TOML"] -git-tree-sha1 = "12ab2a3e7d1e5f523e95b94cd9334ebcf5be220e" +git-tree-sha1 = "cf92130f820a5c92607e2a333d2d86d9bf30a694" uuid = "62b44479-cb7b-5706-934f-f13b2eb2e645" -version = "9.10.0+0" +version = "9.13.0+0" [[deps.CUTENSOR_jll]] deps = ["Artifacts", "CUDA_Runtime_jll", "CompilerSupportLibraries_jll", "JLLWrappers", "LazyArtifacts", "Libdl", "TOML"] -git-tree-sha1 = "2c885279d0da51f9f43b6e868f5c54502ce17b7e" +git-tree-sha1 = "70d3e03b381c8ed5ea385930078d6240b575cd8a" uuid = "35b6c64b-1ee1-5834-92a3-3f624899209a" -version = "2.2.0+0" +version = "2.3.1+0" [[deps.Clang]] deps = ["CEnum", "Clang_jll", "Downloads", "Pkg", "TOML"] @@ -65,9 +65,9 @@ version = "0.19.0" [[deps.Clang_jll]] deps = ["Artifacts", "JLLWrappers", "Libdl", "TOML", "Zlib_jll", "libLLVM_jll"] -git-tree-sha1 = "ebfc8e89823ec2c85ed9fedabe52db149da4c5ec" +git-tree-sha1 = "f85df021a5fd31ac59ea7126232b2875a848544f" uuid = "0ee61d77-7f21-5576-8119-9fcc46b10100" -version = "16.0.6+5" +version = "18.1.7+4" [[deps.CommonMark]] deps = ["PrecompileTools"] @@ -78,7 +78,7 @@ version = "0.9.1" [[deps.CompilerSupportLibraries_jll]] deps = ["Artifacts", "Libdl"] uuid = "e66e0078-7015-5450-92f7-15fbd957f2ae" -version = "1.1.1+0" +version = "1.3.0+1" [[deps.Dates]] deps = ["Printf"] @@ -116,6 +116,11 @@ git-tree-sha1 = "937da4713526b96ac9a178e2035019d3b78ead4a" uuid = "70703baa-626e-46a2-a12c-08ffd08c73b4" version = "0.4.10" +[[deps.JuliaSyntaxHighlighting]] +deps = ["StyledStrings"] +uuid = "ac6e5ff7-fb65-4e79-a425-ec3bc9c03011" +version = "1.12.0" + [[deps.LazyArtifacts]] deps = ["Artifacts", "Pkg"] uuid = "4af54fe1-eca0-43a8-85a7-787d91b784e3" @@ -127,24 +132,24 @@ uuid = "b27032c2-a3e7-50c8-80cd-2d36dbcbfd21" version = "0.6.4" [[deps.LibCURL_jll]] -deps = ["Artifacts", "LibSSH2_jll", "Libdl", "MbedTLS_jll", "Zlib_jll", "nghttp2_jll"] +deps = ["Artifacts", "LibSSH2_jll", "Libdl", "OpenSSL_jll", "Zlib_jll", "nghttp2_jll"] uuid = "deac9b47-8bc7-5906-a0fe-35ac56dc84c0" -version = "8.6.0+0" +version = "8.11.1+1" [[deps.LibGit2]] -deps = ["Base64", "LibGit2_jll", "NetworkOptions", "Printf", "SHA"] +deps = ["LibGit2_jll", "NetworkOptions", "Printf", "SHA"] uuid = "76f85450-5226-5b5a-8eaa-529ad045b433" version = "1.11.0" [[deps.LibGit2_jll]] -deps = ["Artifacts", "LibSSH2_jll", "Libdl", "MbedTLS_jll"] +deps = ["Artifacts", "LibSSH2_jll", "Libdl", "OpenSSL_jll"] uuid = "e37daf67-58a4-590a-8e99-b0245dd2ffc5" -version = "1.7.2+0" +version = "1.9.0+0" [[deps.LibSSH2_jll]] -deps = ["Artifacts", "Libdl", "MbedTLS_jll"] +deps = ["Artifacts", "Libdl", "OpenSSL_jll"] uuid = "29816b5a-b9ab-546f-933c-edad1886dfa8" -version = "1.11.0+1" +version = "1.11.3+1" [[deps.Libdl]] uuid = "8f399da3-3557-5675-b5ff-fb832c97cbdb" @@ -161,27 +166,27 @@ uuid = "56ddb016-857b-54e1-b83d-db4d58db5568" version = "1.11.0" [[deps.Markdown]] -deps = ["Base64"] +deps = ["Base64", "JuliaSyntaxHighlighting", "StyledStrings"] uuid = "d6f4376e-aef5-505a-96c1-9c027394607a" version = "1.11.0" -[[deps.MbedTLS_jll]] -deps = ["Artifacts", "Libdl"] -uuid = "c8ffd9c3-330d-5841-b78e-0817d7145fa1" -version = "2.28.6+0" - [[deps.MozillaCACerts_jll]] uuid = "14a3606d-f60d-562e-9121-12d972cd8159" -version = "2023.12.12" +version = "2025.5.20" [[deps.NetworkOptions]] uuid = "ca575930-c2e3-43a9-ace4-1e988b2c1908" -version = "1.2.0" +version = "1.3.0" + +[[deps.OpenSSL_jll]] +deps = ["Artifacts", "Libdl"] +uuid = "458c3c95-2e84-50aa-8efc-19380b2a3a95" +version = "3.5.1+0" [[deps.Pkg]] deps = ["Artifacts", "Dates", "Downloads", "FileWatching", "LibGit2", "Libdl", "Logging", "Markdown", "Printf", "Random", "SHA", "TOML", "Tar", "UUIDs", "p7zip_jll"] uuid = "44cfe95a-1eb2-52ea-b672-e2afdf69b78f" -version = "1.11.0" +version = "1.12.0" [deps.Pkg.extensions] REPLExt = "REPL" @@ -191,9 +196,9 @@ version = "1.11.0" [[deps.PrecompileTools]] deps = ["Preferences"] -git-tree-sha1 = "5aa36f7049a63a1528fe8f7c3f2113413ffd4e1f" +git-tree-sha1 = "07a921781cab75691315adc645096ed5e370cb77" uuid = "aea7be01-6a6a-4083-8856-8a6e6704d82a" -version = "1.2.1" +version = "1.3.3" [[deps.Preferences]] deps = ["TOML"] @@ -215,6 +220,10 @@ version = "1.11.0" uuid = "ea8e919c-243c-51af-8825-aaa63cd721ce" version = "0.7.0" +[[deps.StyledStrings]] +uuid = "f489334b-da3d-4c2e-b8f0-e476e12c162b" +version = "1.11.0" + [[deps.TOML]] deps = ["Dates"] uuid = "fa267f1f-6049-4f14-aa54-33bafae1ed76" @@ -278,25 +287,25 @@ version = "1.6.0+0" [[deps.Zlib_jll]] deps = ["Libdl"] uuid = "83775a58-1f1d-513f-b197-d71354ab007a" -version = "1.2.13+1" +version = "1.3.1+2" [[deps.cuQuantum_jll]] deps = ["Artifacts", "CUDA_Runtime_jll", "CUTENSOR_jll", "JLLWrappers", "LazyArtifacts", "Libdl", "TOML"] -git-tree-sha1 = "3192cef0d0cac365833c334bb5b4baf6d26dc5cb" +git-tree-sha1 = "3e7921e233c7126e31f0353b8167f283e357ad79" uuid = "b75408ef-6fdf-5d74-b65a-7df000ad18e6" -version = "25.3.0+0" +version = "25.9.0+0" [[deps.libLLVM_jll]] deps = ["Artifacts", "Libdl"] uuid = "8f36deef-c2a5-5394-99ed-8e07531fb29a" -version = "16.0.6+5" +version = "18.1.7+5" [[deps.nghttp2_jll]] deps = ["Artifacts", "Libdl"] uuid = "8e850ede-7688-5339-a07c-302acd2aaf8d" -version = "1.59.0+0" +version = "1.64.0+1" [[deps.p7zip_jll]] deps = ["Artifacts", "Libdl"] uuid = "3f19e933-33d8-53b3-aaab-bd5110c3b7a0" -version = "17.4.0+2" +version = "17.5.0+2"