diff --git a/bindings_generator/src/main.rs b/bindings_generator/src/main.rs index b9dd2c70..e536c24d 100644 --- a/bindings_generator/src/main.rs +++ b/bindings_generator/src/main.rs @@ -35,6 +35,7 @@ fn create_modules() -> Vec { libs: vec!["cudart"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "driver", @@ -55,15 +56,13 @@ fn create_modules() -> Vec { blocklist: Filters { // NOTE: See https://github.com/coreylowman/cudarc/issues/385 types: vec!["^cuCheckpoint.*"], - functions: vec![ - "^cuCheckpoint.*", - "cuDeviceGetNvSciSyncAttributes", - ], + functions: vec!["^cuCheckpoint.*", "cuDeviceGetNvSciSyncAttributes"], vars: vec![], }, libs: vec!["cuda", "nvcuda"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "cublas", @@ -78,6 +77,7 @@ fn create_modules() -> Vec { libs: vec!["cublas"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "cublaslt", @@ -96,6 +96,7 @@ fn create_modules() -> Vec { libs: vec!["cublasLt"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "curand", @@ -108,15 +109,13 @@ fn create_modules() -> Vec { allowlist_recursively: true, blocklist: Filters { types: vec![], - functions: vec![ - "curandGenerateBinomial", - "curandGenerateBinomialMethod", - ], + functions: vec!["curandGenerateBinomial", "curandGenerateBinomialMethod"], vars: vec![], }, libs: vec!["curand"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "nvrtc", @@ -142,6 +141,7 @@ fn create_modules() -> Vec { libs: vec!["nvrtc"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "cudnn", @@ -156,6 +156,7 @@ fn create_modules() -> Vec { libs: vec!["cudnn"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "nccl", @@ -170,6 +171,7 @@ fn create_modules() -> Vec { libs: vec!["nccl"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "cusparse", @@ -226,6 +228,7 @@ fn create_modules() -> Vec { libs: vec!["cusparse"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "cusolver", @@ -238,15 +241,13 @@ fn create_modules() -> Vec { allowlist_recursively: true, blocklist: Filters { types: vec!["^cusolverMg.*"], - functions: vec![ - "^cusolverMg.*", - "^cusolverDnLogger.*", - ], + functions: vec!["^cusolverMg.*", "^cusolverDnLogger.*"], vars: vec!["^cusolverMg.*"], }, libs: vec!["cusolver"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "cusolvermg", @@ -261,6 +262,7 @@ fn create_modules() -> Vec { libs: vec!["cusolverMg"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "cufile", @@ -275,6 +277,7 @@ fn create_modules() -> Vec { libs: vec!["cufile"], clang_args: vec![], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "nvtx", @@ -285,7 +288,7 @@ fn create_modules() -> Vec { vars: vec!["^nvtx.*"], }, allowlist_recursively: true, - blocklist: Filters { + blocklist: Filters { types: vec![], functions: vec!["nvtxInitialize"], vars: vec![], @@ -293,6 +296,7 @@ fn create_modules() -> Vec { libs: vec!["nvToolsExt"], clang_args: vec!["-DNVTX_NO_IMPL=0", "-DNVTX_DECLSPEC="], raw_lines: vec![], + derive_default: true, }, ModuleConfig { cudarc_name: "cupti", @@ -341,10 +345,8 @@ fn create_modules() -> Vec { }, libs: vec!["cupti"], clang_args: vec![], - raw_lines: vec![ - "use crate::driver::sys::*;", - "use crate::runtime::sys::*;", - ], + raw_lines: vec!["use crate::driver::sys::*;", "use crate::runtime::sys::*;"], + derive_default: false, }, ] } @@ -370,6 +372,8 @@ struct ModuleConfig { allowlist_recursively: bool, /// Lines of code to add at the beginning of the generated bindings. raw_lines: Vec<&'static str>, + /// Whether to derive Default implementations for types. + derive_default: bool, } impl ModuleConfig { @@ -399,7 +403,7 @@ impl ModuleConfig { .default_enum_style(bindgen::EnumVariation::Rust { non_exhaustive: false, }) - .derive_default(false) + .derive_default(self.derive_default) .derive_eq(true) .derive_hash(true) .derive_ord(true) @@ -530,7 +534,7 @@ fn create_bindings(modules: &[ModuleConfig], cuda_versions: &[&str]) -> Result<( } else { vec!["cuda_nvcc"] }; - + let archive_pb = multi_progress.add(ProgressBar::new(names.len() as u64)); archive_pb.set_style( ProgressStyle::default_bar().template("{msg} {wide_bar} {pos}/{len} ({eta})")?, diff --git a/src/cublas/sys/mod.rs b/src/cublas/sys/mod.rs index 88fba98c..507b480a 100644 --- a/src/cublas/sys/mod.rs +++ b/src/cublas/sys/mod.rs @@ -459,14 +459,14 @@ pub struct cublasContext { } #[repr(C)] #[repr(align(16))] -#[derive(Debug, Copy, Clone, PartialOrd, PartialEq)] +#[derive(Debug, Default, Copy, Clone, PartialOrd, PartialEq)] pub struct double2 { pub x: f64, pub y: f64, } #[repr(C)] #[repr(align(8))] -#[derive(Debug, Copy, Clone, PartialOrd, PartialEq)] +#[derive(Debug, Default, Copy, Clone, PartialOrd, PartialEq)] pub struct float2 { pub x: f32, pub y: f32, diff --git a/src/cublaslt/sys/mod.rs b/src/cublaslt/sys/mod.rs index 3d36bd30..89c5379c 100644 --- a/src/cublaslt/sys/mod.rs +++ b/src/cublaslt/sys/mod.rs @@ -2695,30 +2695,30 @@ pub struct cublasLtContext { } #[cfg(any(feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cublasLtEmulationDescOpaque_t { pub data: [u64; 8usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cublasLtMatmulAlgo_t { pub data: [u64; 8usize], } #[cfg(any(feature = "cuda-11040"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cublasLtMatmulDescOpaque_t { pub data: [u64; 11usize], } #[cfg(any(feature = "cuda-11050", feature = "cuda-11060", feature = "cuda-11070"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cublasLtMatmulDescOpaque_t { pub data: [u64; 12usize], } #[cfg(any(feature = "cuda-11080", feature = "cuda-12000", feature = "cuda-12010"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cublasLtMatmulDescOpaque_t { pub data: [u64; 23usize], } @@ -2733,7 +2733,7 @@ pub struct cublasLtMatmulDescOpaque_t { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cublasLtMatmulDescOpaque_t { pub data: [u64; 32usize], } @@ -2754,7 +2754,7 @@ pub struct cublasLtMatmulHeuristicResult_t { feature = "cuda-11080" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cublasLtMatmulPreferenceOpaque_t { pub data: [u64; 10usize], } @@ -2771,17 +2771,17 @@ pub struct cublasLtMatmulPreferenceOpaque_t { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cublasLtMatmulPreferenceOpaque_t { pub data: [u64; 8usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cublasLtMatrixLayoutOpaque_t { pub data: [u64; 8usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cublasLtMatrixTransformDescOpaque_t { pub data: [u64; 8usize], } @@ -2789,6 +2789,24 @@ pub struct cublasLtMatrixTransformDescOpaque_t { impl cudaDataType_t { pub const CUDA_R_8F_UE4M3: cudaDataType_t = cudaDataType_t::CUDA_R_8F_E4M3; } +impl Default for _IO_FILE { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cublasLtMatmulHeuristicResult_t { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} #[cfg(not(feature = "dynamic-loading"))] extern "C" { pub fn cublasLtCreate(lightHandle: *mut cublasLtHandle_t) -> cublasStatus_t; diff --git a/src/cudnn/sys/mod.rs b/src/cudnn/sys/mod.rs index e4e4e02f..27bfd429 100644 --- a/src/cudnn/sys/mod.rs +++ b/src/cudnn/sys/mod.rs @@ -1490,7 +1490,7 @@ pub struct cudnnFilterStruct { _unused: [u8; 0], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudnnFractionStruct { pub numerator: i64, pub denominator: i64, @@ -1589,6 +1589,42 @@ impl cudnnStatus_t { pub const CUDNN_STATUS_VERSION_MISMATCH: cudnnStatus_t = cudnnStatus_t::CUDNN_STATUS_SUBLIBRARY_VERSION_MISMATCH; } +impl Default for cudnnConvolutionBwdDataAlgoPerfStruct { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudnnConvolutionBwdFilterAlgoPerfStruct { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudnnConvolutionFwdAlgoPerfStruct { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudnnDebugStruct { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} #[cfg(not(feature = "dynamic-loading"))] extern "C" { pub fn cudnnActivationBackward( diff --git a/src/cufile/sys/mod.rs b/src/cufile/sys/mod.rs index 29a019de..0af3e08e 100644 --- a/src/cufile/sys/mod.rs +++ b/src/cufile/sys/mod.rs @@ -1569,7 +1569,7 @@ pub struct CUfileDescr_t { } #[cfg(any(feature = "cuda-11040", feature = "cuda-11050"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUfileDrvProps { pub nvfs: CUfileDrvProps__bindgen_ty_1, pub fflags: ::core::ffi::c_uint, @@ -1594,7 +1594,7 @@ pub struct CUfileDrvProps { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUfileDrvProps { pub nvfs: CUfileDrvProps__bindgen_ty_1, pub fflags: ::core::ffi::c_uint, @@ -1605,7 +1605,7 @@ pub struct CUfileDrvProps { pub max_batch_io_timeout_msecs: ::core::ffi::c_uint, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUfileDrvProps__bindgen_ty_1 { pub major_version: ::core::ffi::c_uint, pub minor_version: ::core::ffi::c_uint, @@ -1621,7 +1621,7 @@ pub struct CUfileError { pub cu_err: CUresult, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUfileFSOps { pub fs_type: ::core::option::Option< unsafe extern "C" fn(handle: *mut ::core::ffi::c_void) -> *const ::core::ffi::c_char, @@ -1731,14 +1731,14 @@ pub struct CUfileIOParams__bindgen_ty_1__bindgen_ty_1 { } #[cfg(any(feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUfileOpCounter { pub ok: u64, pub err: u64, } #[cfg(any(feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUfilePerGpuStats { pub uuid: [::core::ffi::c_char; 16usize], pub read_bytes: u64, @@ -1773,7 +1773,7 @@ pub struct CUfilePerGpuStats { } #[cfg(any(feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUfileStatsLevel1 { pub read_ops: CUfileOpCounter_t, pub write_ops: CUfileOpCounter_t, @@ -1821,7 +1821,7 @@ pub struct CUfileStatsLevel1 { } #[cfg(any(feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUfileStatsLevel2 { pub basic: CUfileStatsLevel1_t, pub read_size_kb_hist: [u64; 32usize], @@ -1829,7 +1829,7 @@ pub struct CUfileStatsLevel2 { } #[cfg(any(feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUfileStatsLevel3 { pub detailed: CUfileStatsLevel2_t, pub num_gpus: u32, @@ -1858,7 +1858,7 @@ pub struct cufileRDMAInfo { pub desc_str: *const ::core::ffi::c_char, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct sockaddr { pub sa_family: sa_family_t, pub sa_data: [::core::ffi::c_char; 14usize], @@ -1879,11 +1879,143 @@ pub struct sockaddr { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct timespec { pub tv_sec: __time_t, pub tv_nsec: __syscall_slong_t, } +impl Default for CUfileDescr_t { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUfileDescr_t__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUfileError { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUfileIOEvents { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUfileIOParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUfileIOParams__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUfileIOParams__bindgen_ty_1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cufileRDMAInfo { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} #[repr(C)] #[derive(Copy, Clone)] pub union CUfileDescr_t__bindgen_ty_1 { diff --git a/src/cusolver/sys/mod.rs b/src/cusolver/sys/mod.rs index b3e85b6d..80d62d1b 100644 --- a/src/cusolver/sys/mod.rs +++ b/src/cusolver/sys/mod.rs @@ -651,14 +651,14 @@ pub struct cusparseMatDescr { } #[repr(C)] #[repr(align(16))] -#[derive(Debug, Copy, Clone, PartialOrd, PartialEq)] +#[derive(Debug, Default, Copy, Clone, PartialOrd, PartialEq)] pub struct double2 { pub x: f64, pub y: f64, } #[repr(C)] #[repr(align(8))] -#[derive(Debug, Copy, Clone, PartialOrd, PartialEq)] +#[derive(Debug, Default, Copy, Clone, PartialOrd, PartialEq)] pub struct float2 { pub x: f32, pub y: f32, @@ -680,6 +680,29 @@ impl cublasOperation_t { impl cudaDataType_t { pub const CUDA_R_8F_UE4M3: cudaDataType_t = cudaDataType_t::CUDA_R_8F_E4M3; } +#[cfg(any( + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for _IO_FILE { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} #[cfg(not(feature = "dynamic-loading"))] extern "C" { pub fn cusolverDnCCgels( diff --git a/src/cusparse/sys/mod.rs b/src/cusparse/sys/mod.rs index 07837505..65c1cdfa 100644 --- a/src/cusparse/sys/mod.rs +++ b/src/cusparse/sys/mod.rs @@ -1028,14 +1028,14 @@ pub struct cusparseSpVecDescr { } #[repr(C)] #[repr(align(16))] -#[derive(Debug, Copy, Clone, PartialOrd, PartialEq)] +#[derive(Debug, Default, Copy, Clone, PartialOrd, PartialEq)] pub struct double2 { pub x: f64, pub y: f64, } #[repr(C)] #[repr(align(8))] -#[derive(Debug, Copy, Clone, PartialOrd, PartialEq)] +#[derive(Debug, Default, Copy, Clone, PartialOrd, PartialEq)] pub struct float2 { pub x: f32, pub y: f32, @@ -1157,6 +1157,31 @@ impl cusparseSpMVAlg_t { impl cusparseSpMVAlg_t { pub const CUSPARSE_SPMV_CSR_ALG2: cusparseSpMVAlg_t = cusparseSpMVAlg_t::CUSPARSE_CSRMV_ALG2; } +#[cfg(any( + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for _IO_FILE { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} #[cfg(not(feature = "dynamic-loading"))] extern "C" { #[cfg(any( diff --git a/src/driver/sys/mod.rs b/src/driver/sys/mod.rs index 31990aac..ec2ebfc1 100644 --- a/src/driver/sys/mod.rs +++ b/src/driver/sys/mod.rs @@ -6496,14 +6496,14 @@ pub struct CUDA_ARRAY_DESCRIPTOR_st { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_ARRAY_MEMORY_REQUIREMENTS_st { pub size: usize, pub alignment: usize, pub reserved: [::core::ffi::c_uint; 4usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_ARRAY_SPARSE_PROPERTIES_st { pub tileExtent: CUDA_ARRAY_SPARSE_PROPERTIES_st__bindgen_ty_1, pub miptailFirstLevel: ::core::ffi::c_uint, @@ -6512,7 +6512,7 @@ pub struct CUDA_ARRAY_SPARSE_PROPERTIES_st { pub reserved: [::core::ffi::c_uint; 4usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_ARRAY_SPARSE_PROPERTIES_st__bindgen_ty_1 { pub width: ::core::ffi::c_uint, pub height: ::core::ffi::c_uint, @@ -6637,7 +6637,7 @@ pub struct CUDA_EVENT_WAIT_NODE_PARAMS_st { pub event: CUevent, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_EXTERNAL_MEMORY_BUFFER_DESC_st { pub offset: ::core::ffi::c_ulonglong, pub size: ::core::ffi::c_ulonglong, @@ -6697,12 +6697,12 @@ pub struct CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st__bindgen_ty_1 { pub reserved: [::core::ffi::c_uint; 12usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st__bindgen_ty_1__bindgen_ty_1 { pub value: ::core::ffi::c_ulonglong, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st__bindgen_ty_1__bindgen_ty_3 { pub key: ::core::ffi::c_ulonglong, } @@ -6722,12 +6722,12 @@ pub struct CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st__bindgen_ty_1 { pub reserved: [::core::ffi::c_uint; 10usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st__bindgen_ty_1__bindgen_ty_1 { pub value: ::core::ffi::c_ulonglong, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st__bindgen_ty_1__bindgen_ty_3 { pub key: ::core::ffi::c_ulonglong, pub timeoutMs: ::core::ffi::c_uint, @@ -7011,7 +7011,7 @@ pub struct CUDA_MEMCPY_NODE_PARAMS_st { pub copyParams: CUDA_MEMCPY3D, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_MEMSET_NODE_PARAMS_st { pub dst: CUdeviceptr, pub pitch: usize, @@ -7108,12 +7108,12 @@ pub struct CUDA_MEM_ALLOC_NODE_PARAMS_v2_st { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_MEM_FREE_NODE_PARAMS_st { pub dptr: CUdeviceptr, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_POINTER_ATTRIBUTE_P2P_TOKENS_st { pub p2pToken: ::core::ffi::c_ulonglong, pub vaSpaceToken: ::core::ffi::c_uint, @@ -7154,7 +7154,7 @@ pub struct CUDA_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_4 { pub pitchInBytes: usize, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUDA_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_5 { pub reserved: [::core::ffi::c_int; 32usize], } @@ -7210,7 +7210,7 @@ pub struct CUarrayMapInfo_st { pub reserved: [::core::ffi::c_uint; 2usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUarrayMapInfo_st__bindgen_ty_2__bindgen_ty_1 { pub level: ::core::ffi::c_uint, pub layer: ::core::ffi::c_uint, @@ -7222,7 +7222,7 @@ pub struct CUarrayMapInfo_st__bindgen_ty_2__bindgen_ty_1 { pub extentDepth: ::core::ffi::c_uint, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUarrayMapInfo_st__bindgen_ty_2__bindgen_ty_2 { pub layer: ::core::ffi::c_uint, pub offset: ::core::ffi::c_ulonglong, @@ -7269,26 +7269,26 @@ pub struct CUasyncNotificationInfo_st { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUasyncNotificationInfo_st__bindgen_ty_1__bindgen_ty_1 { pub bytesOverBudget: ::core::ffi::c_ulonglong, } #[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUcheckpointCheckpointArgs_st { pub reserved: [cuuint64_t; 8usize], } #[cfg(any(feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUcheckpointGpuPair_st { pub oldUuid: CUuuid, pub newUuid: CUuuid, } #[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUcheckpointLockArgs_st { pub timeoutMs: ::core::ffi::c_uint, pub reserved0: ::core::ffi::c_uint, @@ -7296,7 +7296,7 @@ pub struct CUcheckpointLockArgs_st { } #[cfg(any(feature = "cuda-12080", feature = "cuda-12090"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUcheckpointRestoreArgs_st { pub reserved: [cuuint64_t; 8usize], } @@ -7311,7 +7311,7 @@ pub struct CUcheckpointRestoreArgs_st { } #[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUcheckpointUnlockArgs_st { pub reserved: [cuuint64_t; 8usize], } @@ -7383,20 +7383,20 @@ pub struct CUdevResource_st { feature = "cuda-12090" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUdevSmResource_st { pub smCount: ::core::ffi::c_uint, } #[cfg(any(feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUdevSmResource_st { pub smCount: ::core::ffi::c_uint, pub minSmPartitionSize: ::core::ffi::c_uint, pub smCoscheduledAlignment: ::core::ffi::c_uint, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUdevprop_st { pub maxThreadsPerBlock: ::core::ffi::c_int, pub maxThreadsDim: [::core::ffi::c_int; 3usize], @@ -7421,7 +7421,7 @@ pub struct CUexecAffinityParam_st { pub param: CUexecAffinityParam_st__bindgen_ty_1, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUexecAffinitySmCount_st { pub val: ::core::ffi::c_uint, } @@ -7437,7 +7437,7 @@ pub struct CUextSemaphore_st { } #[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUextent3D_st { pub width: usize, pub height: usize, @@ -7471,7 +7471,7 @@ pub struct CUgraphDeviceUpdatableNode_st { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUgraphEdgeData_st { pub from_port: ::core::ffi::c_uchar, pub to_port: ::core::ffi::c_uchar, @@ -7589,7 +7589,7 @@ pub struct CUkern_st { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUlaunchAttributeValue_union__bindgen_ty_1 { pub x: ::core::ffi::c_uint, pub y: ::core::ffi::c_uint, @@ -7639,7 +7639,7 @@ pub struct CUlaunchAttributeValue_union__bindgen_ty_4 { } #[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUlaunchAttributeValue_union__bindgen_ty_4 { pub x: ::core::ffi::c_uint, pub y: ::core::ffi::c_uint, @@ -7712,7 +7712,7 @@ pub struct CUlaunchConfig_st { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUlaunchMemSyncDomainMap_st { pub default_: ::core::ffi::c_uchar, pub remote: ::core::ffi::c_uchar, @@ -7781,7 +7781,7 @@ pub struct CUmemAllocationProp_st { pub allocFlags: CUmemAllocationProp_st__bindgen_ty_1, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUmemAllocationProp_st__bindgen_ty_1 { pub compressionType: ::core::ffi::c_uchar, pub gpuDirectRDMACapable: ::core::ffi::c_uchar, @@ -7935,7 +7935,7 @@ pub struct CUmod_st { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUmulticastObjectProp_st { pub numDevices: ::core::ffi::c_uint, pub size: usize, @@ -7944,7 +7944,7 @@ pub struct CUmulticastObjectProp_st { } #[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUoffset3D_st { pub x: usize, pub y: usize, @@ -8041,7 +8041,7 @@ pub struct CUuserObject_st { _unused: [u8; 0], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUuuid_st { pub bytes: [::core::ffi::c_char; 16usize], } @@ -8081,6 +8081,1283 @@ impl CUmemLocationType_enum { pub const CU_MEM_LOCATION_TYPE_NONE: CUmemLocationType_enum = CUmemLocationType_enum::CU_MEM_LOCATION_TYPE_INVALID; } +impl Default for CUDA_ARRAY3D_DESCRIPTOR_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_ARRAY_DESCRIPTOR_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010" +))] +impl Default for CUDA_BATCH_MEM_OP_NODE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_BATCH_MEM_OP_NODE_PARAMS_v1_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_BATCH_MEM_OP_NODE_PARAMS_v2_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_CHILD_GRAPH_NODE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_CONDITIONAL_NODE_PARAMS { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_EVENT_RECORD_NODE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_EVENT_WAIT_NODE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st__bindgen_ty_1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_MEMORY_MIPMAPPED_ARRAY_DESC_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_SEMAPHORE_HANDLE_DESC_st__bindgen_ty_1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_SEMAPHORE_SIGNAL_PARAMS_st__bindgen_ty_1__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXTERNAL_SEMAPHORE_WAIT_PARAMS_st__bindgen_ty_1__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_EXT_SEM_SIGNAL_NODE_PARAMS_v2_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_EXT_SEM_WAIT_NODE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_EXT_SEM_WAIT_NODE_PARAMS_v2_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_GRAPH_INSTANTIATE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_HOST_NODE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_HOST_NODE_PARAMS_v2_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_KERNEL_NODE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_KERNEL_NODE_PARAMS_v2_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_KERNEL_NODE_PARAMS_v3_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_LAUNCH_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_MEMCPY2D_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for CUDA_MEMCPY3D_BATCH_OP_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_MEMCPY3D_PEER_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_MEMCPY3D_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_MEMCPY_NODE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_MEMSET_NODE_PARAMS_v2_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11040", + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010" +))] +impl Default for CUDA_MEM_ALLOC_NODE_PARAMS_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_MEM_ALLOC_NODE_PARAMS_v1_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUDA_MEM_ALLOC_NODE_PARAMS_v2_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_RESOURCE_DESC_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_RESOURCE_DESC_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_3 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_4 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_RESOURCE_VIEW_DESC_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUDA_TEXTURE_DESC_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUaccessPolicyWindow_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUarrayMapInfo_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUarrayMapInfo_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUarrayMapInfo_st__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUarrayMapInfo_st__bindgen_ty_3 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUasyncNotificationInfo_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUasyncNotificationInfo_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-13000"))] +impl Default for CUcheckpointRestoreArgs_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUctxCigParam_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUctxCreateParams_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUdevResource_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUdevResource_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUexecAffinityParam_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUexecAffinityParam_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUgraphExecUpdateResultInfo_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUgraphNodeParams_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUgraphNodeParams_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUipcEventHandle_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUipcMemHandle_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11040", + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070" +))] +impl Default for CUkernelNodeAttrValue_union { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUlaunchAttributeValue_union { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUlaunchAttributeValue_union__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUlaunchAttributeValue_union__bindgen_ty_3 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12040", feature = "cuda-12050", feature = "cuda-12060"))] +impl Default for CUlaunchAttributeValue_union__bindgen_ty_4 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for CUlaunchAttributeValue_union__bindgen_ty_5 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUlaunchAttribute_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUlaunchConfig_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUlibraryHostUniversalFunctionAndDataTable_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUmemAccessDesc_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUmemAllocationProp_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for CUmemDecompressParams_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUmemFabricHandle_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUmemLocation_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUmemPoolProps_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUmemPoolPtrExportData_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for CUmemcpy3DOperand_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for CUmemcpy3DOperand_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for CUmemcpy3DOperand_st__bindgen_ty_1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for CUmemcpy3DOperand_st__bindgen_ty_1__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for CUmemcpyAttributes_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11040", + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070" +))] +impl Default for CUstreamAttrValue_union { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUstreamBatchMemOpParams_union { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUstreamBatchMemOpParams_union_CUstreamMemOpFlushRemoteWritesParams_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUstreamBatchMemOpParams_union_CUstreamMemOpMemoryBarrierParams_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUstreamBatchMemOpParams_union_CUstreamMemOpWaitValueParams_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUstreamBatchMemOpParams_union_CUstreamMemOpWaitValueParams_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUstreamBatchMemOpParams_union_CUstreamMemOpWriteValueParams_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for CUstreamBatchMemOpParams_union_CUstreamMemOpWriteValueParams_st__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for CUtensorMap_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} #[repr(C)] #[derive(Copy, Clone)] pub union CUDA_EXTERNAL_MEMORY_HANDLE_DESC_st__bindgen_ty_1 { diff --git a/src/nccl/sys/mod.rs b/src/nccl/sys/mod.rs index fafd8df2..7054371b 100644 --- a/src/nccl/sys/mod.rs +++ b/src/nccl/sys/mod.rs @@ -95,7 +95,7 @@ pub struct ncclConfig_v22800 { pub nvlinkCentricSched: ::core::ffi::c_int, } #[repr(C)] -#[derive(Debug, Copy, Clone, PartialOrd, PartialEq)] +#[derive(Debug, Default, Copy, Clone, PartialOrd, PartialEq)] pub struct ncclSimInfo_v22200 { pub size: usize, pub magic: ::core::ffi::c_uint, @@ -127,6 +127,24 @@ impl ncclDataType_t { impl ncclDataType_t { pub const ncclInt: ncclDataType_t = ncclDataType_t::ncclInt32; } +impl Default for ncclConfig_v22800 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for ncclUniqueId { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} #[cfg(not(feature = "dynamic-loading"))] extern "C" { pub fn ncclAllGather( diff --git a/src/nvtx/sys/mod.rs b/src/nvtx/sys/mod.rs index aa504a8d..418c0490 100644 --- a/src/nvtx/sys/mod.rs +++ b/src/nvtx/sys/mod.rs @@ -503,6 +503,51 @@ pub struct nvtxSyncUser { pub struct nvtxSyncUserAttributes_v0 { _unused: [u8; 0], } +impl Default for nvtxEventAttributes_v2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for nvtxEventAttributes_v2_payload_t { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for nvtxMessageValue_t { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for nvtxResourceAttributes_v0 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for nvtxResourceAttributes_v0_identifier_t { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} #[repr(C)] #[derive(Copy, Clone)] pub union nvtxEventAttributes_v2_payload_t { diff --git a/src/runtime/sys/mod.rs b/src/runtime/sys/mod.rs index 1670835a..6c56329a 100644 --- a/src/runtime/sys/mod.rs +++ b/src/runtime/sys/mod.rs @@ -4490,7 +4490,7 @@ pub struct CUuserObject_st { _unused: [u8; 0], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct CUuuid_st { pub bytes: [::core::ffi::c_char; 16usize], } @@ -4524,14 +4524,14 @@ pub struct cudaArray { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaArrayMemoryRequirements { pub size: usize, pub alignment: usize, pub reserved: [::core::ffi::c_uint; 4usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaArraySparseProperties { pub tileExtent: cudaArraySparseProperties__bindgen_ty_1, pub miptailFirstLevel: ::core::ffi::c_uint, @@ -4540,7 +4540,7 @@ pub struct cudaArraySparseProperties { pub reserved: [::core::ffi::c_uint; 4usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaArraySparseProperties__bindgen_ty_1 { pub width: ::core::ffi::c_uint, pub height: ::core::ffi::c_uint, @@ -4582,7 +4582,7 @@ pub struct cudaAsyncNotificationInfo { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaAsyncNotificationInfo__bindgen_ty_1__bindgen_ty_1 { pub bytesOverBudget: ::core::ffi::c_ulonglong, } @@ -5256,7 +5256,7 @@ pub struct cudaEventWaitNodeParams { pub event: cudaEvent_t, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExtent { pub width: usize, pub height: usize, @@ -5279,7 +5279,7 @@ pub struct cudaExtent { feature = "cuda-12090" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExternalMemoryBufferDesc { pub offset: ::core::ffi::c_ulonglong, pub size: ::core::ffi::c_ulonglong, @@ -5287,7 +5287,7 @@ pub struct cudaExternalMemoryBufferDesc { } #[cfg(any(feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExternalMemoryBufferDesc { pub offset: ::core::ffi::c_ulonglong, pub size: ::core::ffi::c_ulonglong, @@ -5448,12 +5448,12 @@ pub struct cudaExternalSemaphoreSignalParams__bindgen_ty_1 { pub reserved: [::core::ffi::c_uint; 12usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExternalSemaphoreSignalParams__bindgen_ty_1__bindgen_ty_1 { pub value: ::core::ffi::c_ulonglong, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExternalSemaphoreSignalParams__bindgen_ty_1__bindgen_ty_3 { pub key: ::core::ffi::c_ulonglong, } @@ -5516,7 +5516,7 @@ pub struct cudaExternalSemaphoreSignalParams_v1__bindgen_ty_1 { feature = "cuda-12090" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExternalSemaphoreSignalParams_v1__bindgen_ty_1__bindgen_ty_1 { pub value: ::core::ffi::c_ulonglong, } @@ -5536,7 +5536,7 @@ pub struct cudaExternalSemaphoreSignalParams_v1__bindgen_ty_1__bindgen_ty_1 { feature = "cuda-12090" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExternalSemaphoreSignalParams_v1__bindgen_ty_1__bindgen_ty_3 { pub key: ::core::ffi::c_ulonglong, } @@ -5580,12 +5580,12 @@ pub struct cudaExternalSemaphoreWaitParams__bindgen_ty_1 { pub reserved: [::core::ffi::c_uint; 10usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExternalSemaphoreWaitParams__bindgen_ty_1__bindgen_ty_1 { pub value: ::core::ffi::c_ulonglong, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExternalSemaphoreWaitParams__bindgen_ty_1__bindgen_ty_3 { pub key: ::core::ffi::c_ulonglong, pub timeoutMs: ::core::ffi::c_uint, @@ -5649,7 +5649,7 @@ pub struct cudaExternalSemaphoreWaitParams_v1__bindgen_ty_1 { feature = "cuda-12090" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExternalSemaphoreWaitParams_v1__bindgen_ty_1__bindgen_ty_1 { pub value: ::core::ffi::c_ulonglong, } @@ -5669,7 +5669,7 @@ pub struct cudaExternalSemaphoreWaitParams_v1__bindgen_ty_1__bindgen_ty_1 { feature = "cuda-12090" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaExternalSemaphoreWaitParams_v1__bindgen_ty_1__bindgen_ty_3 { pub key: ::core::ffi::c_ulonglong, pub timeoutMs: ::core::ffi::c_uint, @@ -5682,7 +5682,7 @@ pub struct cudaExternalSemaphoreWaitParams_v1__bindgen_ty_1__bindgen_ty_3 { feature = "cuda-11080" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaFuncAttributes { pub sharedSizeBytes: usize, pub constSizeBytes: usize, @@ -5708,7 +5708,7 @@ pub struct cudaFuncAttributes { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaFuncAttributes { pub sharedSizeBytes: usize, pub constSizeBytes: usize, @@ -5738,7 +5738,7 @@ pub struct cudaFuncAttributes { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaGraphEdgeData_st { pub from_port: ::core::ffi::c_uchar, pub to_port: ::core::ffi::c_uchar, @@ -5913,7 +5913,7 @@ pub struct cudaKernelNodeParamsV2 { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaLaunchAttributeValue__bindgen_ty_1 { pub x: ::core::ffi::c_uint, pub y: ::core::ffi::c_uint, @@ -5953,7 +5953,7 @@ pub struct cudaLaunchAttributeValue__bindgen_ty_3 { } #[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaLaunchAttributeValue__bindgen_ty_3 { pub x: ::core::ffi::c_uint, pub y: ::core::ffi::c_uint, @@ -6036,7 +6036,7 @@ pub struct cudaLaunchConfig_st { feature = "cuda-13000" ))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaLaunchMemSyncDomainMap_st { pub default_: ::core::ffi::c_uchar, pub remote: ::core::ffi::c_uchar, @@ -6313,7 +6313,7 @@ pub struct cudaMipmappedArray { } #[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaOffset3D { pub x: usize, pub y: usize, @@ -6362,7 +6362,7 @@ pub struct cudaPointerAttributes { pub reserved: [::core::ffi::c_long; 8usize], } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaPos { pub x: usize, pub y: usize, @@ -6426,7 +6426,7 @@ pub struct cudaResourceDesc__bindgen_ty_1__bindgen_ty_4 { } #[cfg(any(feature = "cuda-13000"))] #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct cudaResourceDesc__bindgen_ty_1__bindgen_ty_5 { pub reserved: [::core::ffi::c_int; 32usize], } @@ -6581,7 +6581,7 @@ pub struct cudalibraryHostUniversalFunctionAndDataTable { pub dataWindowSize: usize, } #[repr(C)] -#[derive(Debug, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] +#[derive(Debug, Default, Copy, Clone, Hash, PartialOrd, Ord, PartialEq, Eq)] pub struct dim3 { pub x: ::core::ffi::c_uint, pub y: ::core::ffi::c_uint, @@ -6650,6 +6650,1217 @@ impl cudaMemLocationType { pub const cudaMemLocationTypeNone: cudaMemLocationType = cudaMemLocationType::cudaMemLocationTypeInvalid; } +impl Default for cudaAccessPolicyWindow { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaAsyncNotificationInfo { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaAsyncNotificationInfo__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaChannelFormatDesc { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaChildGraphNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaConditionalNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaDeviceProp { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaEventRecordNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaEventWaitNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalMemoryHandleDesc { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalMemoryHandleDesc__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalMemoryHandleDesc__bindgen_ty_1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalMemoryMipmappedArrayDesc { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreHandleDesc { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreHandleDesc__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreHandleDesc__bindgen_ty_1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreSignalNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaExternalSemaphoreSignalNodeParamsV2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreSignalParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreSignalParams__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreSignalParams__bindgen_ty_1__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090" +))] +impl Default for cudaExternalSemaphoreSignalParams_v1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090" +))] +impl Default for cudaExternalSemaphoreSignalParams_v1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090" +))] +impl Default for cudaExternalSemaphoreSignalParams_v1__bindgen_ty_1__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreWaitNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaExternalSemaphoreWaitNodeParamsV2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreWaitParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreWaitParams__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaExternalSemaphoreWaitParams__bindgen_ty_1__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090" +))] +impl Default for cudaExternalSemaphoreWaitParams_v1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090" +))] +impl Default for cudaExternalSemaphoreWaitParams_v1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090" +))] +impl Default for cudaExternalSemaphoreWaitParams_v1__bindgen_ty_1__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaGraphExecUpdateResultInfo_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaGraphInstantiateParams_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaGraphKernelNodeUpdate { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaGraphKernelNodeUpdate__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaGraphKernelNodeUpdate__bindgen_ty_1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaGraphNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaGraphNodeParams__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaHostNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaHostNodeParamsV2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaIpcEventHandle_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaIpcMemHandle_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11040", + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070" +))] +impl Default for cudaKernelNodeAttrValue { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaKernelNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaKernelNodeParamsV2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaLaunchAttributeValue { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaLaunchAttributeValue__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060" +))] +impl Default for cudaLaunchAttributeValue__bindgen_ty_3 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaLaunchAttributeValue__bindgen_ty_4 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for cudaLaunchAttributeValue__bindgen_ty_5 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaLaunchAttribute_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaLaunchConfig_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11040", + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080", + feature = "cuda-12000", + feature = "cuda-12010", + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090" +))] +impl Default for cudaLaunchParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaMemAccessDesc { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaMemAllocNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaMemAllocNodeParamsV2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaMemFabricHandle_st { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaMemFreeNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaMemLocation { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaMemPoolProps { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaMemPoolPtrExportData { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for cudaMemcpy3DBatchOp { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for cudaMemcpy3DOperand { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for cudaMemcpy3DOperand__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for cudaMemcpy3DOperand__bindgen_ty_1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for cudaMemcpy3DOperand__bindgen_ty_1__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaMemcpy3DParms { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaMemcpy3DPeerParms { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for cudaMemcpyAttributes { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaMemcpyNodeParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaMemsetParams { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-12020", + feature = "cuda-12030", + feature = "cuda-12040", + feature = "cuda-12050", + feature = "cuda-12060", + feature = "cuda-12080", + feature = "cuda-12090", + feature = "cuda-13000" +))] +impl Default for cudaMemsetParamsV2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaPitchedPtr { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaPointerAttributes { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaResourceDesc { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaResourceDesc__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaResourceDesc__bindgen_ty_1__bindgen_ty_1 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaResourceDesc__bindgen_ty_1__bindgen_ty_2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaResourceDesc__bindgen_ty_1__bindgen_ty_3 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaResourceDesc__bindgen_ty_1__bindgen_ty_4 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaResourceViewDesc { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11040", + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070" +))] +impl Default for cudaStreamAttrValue { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +impl Default for cudaTextureDesc { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-11080"))] +impl Default for cudaTextureDesc_v2 { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any(feature = "cuda-12080", feature = "cuda-12090", feature = "cuda-13000"))] +impl Default for cudalibraryHostUniversalFunctionAndDataTable { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11040", + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080" +))] +impl Default for surfaceReference { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} +#[cfg(any( + feature = "cuda-11040", + feature = "cuda-11050", + feature = "cuda-11060", + feature = "cuda-11070", + feature = "cuda-11080" +))] +impl Default for textureReference { + fn default() -> Self { + let mut s = ::core::mem::MaybeUninit::::uninit(); + unsafe { + ::core::ptr::write_bytes(s.as_mut_ptr(), 0, 1); + s.assume_init() + } + } +} #[cfg(any( feature = "cuda-12040", feature = "cuda-12050",