#[repr(C)]
#[derive(Copy, Clone, Debug, Default, Eq, Hash, Ord, PartialEq, PartialOrd)]
pub struct __BindgenBitfieldUnit<Storage> {
storage: Storage,
}
impl<Storage> __BindgenBitfieldUnit<Storage> {
#[inline]
pub const fn new(storage: Storage) -> Self {
Self { storage }
}
}
impl<Storage> __BindgenBitfieldUnit<Storage>
where
Storage: AsRef<[u8]> + AsMut<[u8]>,
{
#[inline]
fn extract_bit(byte: u8, index: usize) -> bool {
let bit_index = if cfg!(target_endian = "big") {
7 - (index % 8)
} else {
index % 8
};
let mask = 1 << bit_index;
byte & mask == mask
}
#[inline]
pub fn get_bit(&self, index: usize) -> bool {
debug_assert!(index / 8 < self.storage.as_ref().len());
let byte_index = index / 8;
let byte = self.storage.as_ref()[byte_index];
Self::extract_bit(byte, index)
}
#[inline]
pub unsafe fn raw_get_bit(this: *const Self, index: usize) -> bool {
debug_assert!(index / 8 < core::mem::size_of::<Storage>());
let byte_index = index / 8;
let byte = *(core::ptr::addr_of!((*this).storage) as *const u8).offset(byte_index as isize);
Self::extract_bit(byte, index)
}
#[inline]
fn change_bit(byte: u8, index: usize, val: bool) -> u8 {
let bit_index = if cfg!(target_endian = "big") {
7 - (index % 8)
} else {
index % 8
};
let mask = 1 << bit_index;
if val {
byte | mask
} else {
byte & !mask
}
}
#[inline]
pub fn set_bit(&mut self, index: usize, val: bool) {
debug_assert!(index / 8 < self.storage.as_ref().len());
let byte_index = index / 8;
let byte = &mut self.storage.as_mut()[byte_index];
*byte = Self::change_bit(*byte, index, val);
}
#[inline]
pub unsafe fn raw_set_bit(this: *mut Self, index: usize, val: bool) {
debug_assert!(index / 8 < core::mem::size_of::<Storage>());
let byte_index = index / 8;
let byte =
(core::ptr::addr_of_mut!((*this).storage) as *mut u8).offset(byte_index as isize);
*byte = Self::change_bit(*byte, index, val);
}
#[inline]
pub fn get(&self, bit_offset: usize, bit_width: u8) -> u64 {
debug_assert!(bit_width <= 64);
debug_assert!(bit_offset / 8 < self.storage.as_ref().len());
debug_assert!((bit_offset + (bit_width as usize)) / 8 <= self.storage.as_ref().len());
let mut val = 0;
for i in 0..(bit_width as usize) {
if self.get_bit(i + bit_offset) {
let index = if cfg!(target_endian = "big") {
bit_width as usize - 1 - i
} else {
i
};
val |= 1 << index;
}
}
val
}
#[inline]
pub unsafe fn raw_get(this: *const Self, bit_offset: usize, bit_width: u8) -> u64 {
debug_assert!(bit_width <= 64);
debug_assert!(bit_offset / 8 < core::mem::size_of::<Storage>());
debug_assert!((bit_offset + (bit_width as usize)) / 8 <= core::mem::size_of::<Storage>());
let mut val = 0;
for i in 0..(bit_width as usize) {
if Self::raw_get_bit(this, i + bit_offset) {
let index = if cfg!(target_endian = "big") {
bit_width as usize - 1 - i
} else {
i
};
val |= 1 << index;
}
}
val
}
#[inline]
pub fn set(&mut self, bit_offset: usize, bit_width: u8, val: u64) {
debug_assert!(bit_width <= 64);
debug_assert!(bit_offset / 8 < self.storage.as_ref().len());
debug_assert!((bit_offset + (bit_width as usize)) / 8 <= self.storage.as_ref().len());
for i in 0..(bit_width as usize) {
let mask = 1 << i;
let val_bit_is_set = val & mask == mask;
let index = if cfg!(target_endian = "big") {
bit_width as usize - 1 - i
} else {
i
};
self.set_bit(index + bit_offset, val_bit_is_set);
}
}
#[inline]
pub unsafe fn raw_set(this: *mut Self, bit_offset: usize, bit_width: u8, val: u64) {
debug_assert!(bit_width <= 64);
debug_assert!(bit_offset / 8 < core::mem::size_of::<Storage>());
debug_assert!((bit_offset + (bit_width as usize)) / 8 <= core::mem::size_of::<Storage>());
for i in 0..(bit_width as usize) {
let mask = 1 << i;
let val_bit_is_set = val & mask == mask;
let index = if cfg!(target_endian = "big") {
bit_width as usize - 1 - i
} else {
i
};
Self::raw_set_bit(this, index + bit_offset, val_bit_is_set);
}
}
}
pub const HIP_VERSION_MAJOR: u32 = 7;
pub const HIP_VERSION_MINOR: u32 = 1;
pub const HIP_VERSION_PATCH: u32 = 52802;
pub const HIP_VERSION_GITHASH: &[u8; 1] = b"\0";
pub const HIP_VERSION_BUILD_ID: u32 = 0;
pub const HIP_VERSION_BUILD_NAME: &[u8; 1] = b"\0";
pub const HIP_VERSION: u32 = 70152802;
pub const HIP_TRSA_OVERRIDE_FORMAT: u32 = 1;
pub const HIP_TRSF_READ_AS_INTEGER: u32 = 1;
pub const HIP_TRSF_NORMALIZED_COORDINATES: u32 = 2;
pub const HIP_TRSF_SRGB: u32 = 16;
pub const hipTextureType1D: u32 = 1;
pub const hipTextureType2D: u32 = 2;
pub const hipTextureType3D: u32 = 3;
pub const hipTextureTypeCubemap: u32 = 12;
pub const hipTextureType1DLayered: u32 = 241;
pub const hipTextureType2DLayered: u32 = 242;
pub const hipTextureTypeCubemapLayered: u32 = 252;
pub const HIP_IMAGE_OBJECT_SIZE_DWORD: u32 = 12;
pub const HIP_SAMPLER_OBJECT_SIZE_DWORD: u32 = 8;
pub const HIP_SAMPLER_OBJECT_OFFSET_DWORD: u32 = 12;
pub const HIP_TEXTURE_OBJECT_SIZE_DWORD: u32 = 20;
pub const HIP_DEPRECATED_MSG : & [u8 ; 189] = b"This API is marked as deprecated and might not be supported in future releases. For more details please refer https://github.com/ROCm/HIP/blob/develop/docs/reference/deprecated_api_list.md\0" ;
pub const hipIpcMemLazyEnablePeerAccess: u32 = 1;
pub const HIP_IPC_HANDLE_SIZE: u32 = 64;
pub const hipStreamDefault: u32 = 0;
pub const hipStreamNonBlocking: u32 = 1;
pub const hipEventDefault: u32 = 0;
pub const hipEventBlockingSync: u32 = 1;
pub const hipEventDisableTiming: u32 = 2;
pub const hipEventInterprocess: u32 = 4;
pub const hipEventRecordDefault: u32 = 0;
pub const hipEventRecordExternal: u32 = 1;
pub const hipEventWaitDefault: u32 = 0;
pub const hipEventWaitExternal: u32 = 1;
pub const hipEventDisableSystemFence: u32 = 536870912;
pub const hipEventReleaseToDevice: u32 = 1073741824;
pub const hipEventReleaseToSystem: u32 = 2147483648;
pub const hipEnableDefault: u32 = 0;
pub const hipEnableLegacyStream: u32 = 1;
pub const hipEnablePerThreadDefaultStream: u32 = 2;
pub const hipHostAllocDefault: u32 = 0;
pub const hipHostMallocDefault: u32 = 0;
pub const hipHostAllocPortable: u32 = 1;
pub const hipHostMallocPortable: u32 = 1;
pub const hipHostAllocMapped: u32 = 2;
pub const hipHostMallocMapped: u32 = 2;
pub const hipHostAllocWriteCombined: u32 = 4;
pub const hipHostMallocWriteCombined: u32 = 4;
pub const hipHostMallocUncached: u32 = 268435456;
pub const hipHostAllocUncached: u32 = 268435456;
pub const hipHostMallocNumaUser: u32 = 536870912;
pub const hipHostMallocCoherent: u32 = 1073741824;
pub const hipHostMallocNonCoherent: u32 = 2147483648;
pub const hipMemAttachGlobal: u32 = 1;
pub const hipMemAttachHost: u32 = 2;
pub const hipMemAttachSingle: u32 = 4;
pub const hipDeviceMallocDefault: u32 = 0;
pub const hipDeviceMallocFinegrained: u32 = 1;
pub const hipMallocSignalMemory: u32 = 2;
pub const hipDeviceMallocUncached: u32 = 3;
pub const hipDeviceMallocContiguous: u32 = 4;
pub const hipHostRegisterDefault: u32 = 0;
pub const hipHostRegisterPortable: u32 = 1;
pub const hipHostRegisterMapped: u32 = 2;
pub const hipHostRegisterIoMemory: u32 = 4;
pub const hipHostRegisterReadOnly: u32 = 8;
pub const hipExtHostRegisterCoarseGrained: u32 = 8;
pub const hipExtHostRegisterUncached: u32 = 2147483648;
pub const hipDeviceScheduleAuto: u32 = 0;
pub const hipDeviceScheduleSpin: u32 = 1;
pub const hipDeviceScheduleYield: u32 = 2;
pub const hipDeviceScheduleBlockingSync: u32 = 4;
pub const hipDeviceScheduleMask: u32 = 7;
pub const hipDeviceMapHost: u32 = 8;
pub const hipDeviceLmemResizeToMax: u32 = 16;
pub const hipArrayDefault: u32 = 0;
pub const hipArrayLayered: u32 = 1;
pub const hipArraySurfaceLoadStore: u32 = 2;
pub const hipArrayCubemap: u32 = 4;
pub const hipArrayTextureGather: u32 = 8;
pub const hipOccupancyDefault: u32 = 0;
pub const hipOccupancyDisableCachingOverride: u32 = 1;
pub const hipCooperativeLaunchMultiDeviceNoPreSync: u32 = 1;
pub const hipCooperativeLaunchMultiDeviceNoPostSync: u32 = 2;
pub const hipExtAnyOrderLaunch: u32 = 1;
pub const hipStreamWaitValueGte: u32 = 0;
pub const hipStreamWaitValueEq: u32 = 1;
pub const hipStreamWaitValueAnd: u32 = 2;
pub const hipStreamWaitValueNor: u32 = 3;
pub const hipExternalMemoryDedicated: u32 = 1;
pub const hipGraphKernelNodePortDefault: u32 = 0;
pub const hipGraphKernelNodePortLaunchCompletion: u32 = 2;
pub const hipGraphKernelNodePortProgrammatic: u32 = 1;
pub const hipJitOption_hipJitOptionMaxRegisters: hipJitOption = 0;
pub const hipJitOption_hipJitOptionThreadsPerBlock: hipJitOption = 1;
pub const hipJitOption_hipJitOptionWallTime: hipJitOption = 2;
pub const hipJitOption_hipJitOptionInfoLogBuffer: hipJitOption = 3;
pub const hipJitOption_hipJitOptionInfoLogBufferSizeBytes: hipJitOption = 4;
pub const hipJitOption_hipJitOptionErrorLogBuffer: hipJitOption = 5;
pub const hipJitOption_hipJitOptionErrorLogBufferSizeBytes: hipJitOption = 6;
pub const hipJitOption_hipJitOptionOptimizationLevel: hipJitOption = 7;
pub const hipJitOption_hipJitOptionTargetFromContext: hipJitOption = 8;
pub const hipJitOption_hipJitOptionTarget: hipJitOption = 9;
pub const hipJitOption_hipJitOptionFallbackStrategy: hipJitOption = 10;
pub const hipJitOption_hipJitOptionGenerateDebugInfo: hipJitOption = 11;
pub const hipJitOption_hipJitOptionLogVerbose: hipJitOption = 12;
pub const hipJitOption_hipJitOptionGenerateLineInfo: hipJitOption = 13;
pub const hipJitOption_hipJitOptionCacheMode: hipJitOption = 14;
pub const hipJitOption_hipJitOptionSm3xOpt: hipJitOption = 15;
pub const hipJitOption_hipJitOptionFastCompile: hipJitOption = 16;
pub const hipJitOption_hipJitOptionGlobalSymbolNames: hipJitOption = 17;
pub const hipJitOption_hipJitOptionGlobalSymbolAddresses: hipJitOption = 18;
pub const hipJitOption_hipJitOptionGlobalSymbolCount: hipJitOption = 19;
pub const hipJitOption_hipJitOptionLto: hipJitOption = 20;
pub const hipJitOption_hipJitOptionFtz: hipJitOption = 21;
pub const hipJitOption_hipJitOptionPrecDiv: hipJitOption = 22;
pub const hipJitOption_hipJitOptionPrecSqrt: hipJitOption = 23;
pub const hipJitOption_hipJitOptionFma: hipJitOption = 24;
pub const hipJitOption_hipJitOptionPositionIndependentCode: hipJitOption = 25;
pub const hipJitOption_hipJitOptionMinCTAPerSM: hipJitOption = 26;
pub const hipJitOption_hipJitOptionMaxThreadsPerBlock: hipJitOption = 27;
pub const hipJitOption_hipJitOptionOverrideDirectiveValues: hipJitOption = 28;
pub const hipJitOption_hipJitOptionNumOptions: hipJitOption = 29;
pub const hipJitOption_hipJitOptionIRtoISAOptExt: hipJitOption = 10000;
pub const hipJitOption_hipJitOptionIRtoISAOptCountExt: hipJitOption = 10001;
pub type hipJitOption = ::std::os::raw::c_uint;
pub const hipJitInputType_hipJitInputCubin: hipJitInputType = 0;
pub const hipJitInputType_hipJitInputPtx: hipJitInputType = 1;
pub const hipJitInputType_hipJitInputFatBinary: hipJitInputType = 2;
pub const hipJitInputType_hipJitInputObject: hipJitInputType = 3;
pub const hipJitInputType_hipJitInputLibrary: hipJitInputType = 4;
pub const hipJitInputType_hipJitInputNvvm: hipJitInputType = 5;
pub const hipJitInputType_hipJitNumLegacyInputTypes: hipJitInputType = 6;
pub const hipJitInputType_hipJitInputLLVMBitcode: hipJitInputType = 100;
pub const hipJitInputType_hipJitInputLLVMBundledBitcode: hipJitInputType = 101;
pub const hipJitInputType_hipJitInputLLVMArchivesOfBundledBitcode: hipJitInputType = 102;
pub const hipJitInputType_hipJitInputSpirv: hipJitInputType = 103;
pub const hipJitInputType_hipJitNumInputTypes: hipJitInputType = 10;
pub type hipJitInputType = ::std::os::raw::c_uint;
pub const hipJitCacheMode_hipJitCacheOptionNone: hipJitCacheMode = 0;
pub const hipJitCacheMode_hipJitCacheOptionCG: hipJitCacheMode = 1;
pub const hipJitCacheMode_hipJitCacheOptionCA: hipJitCacheMode = 2;
pub type hipJitCacheMode = ::std::os::raw::c_uint;
pub const hipJitFallback_hipJitPreferPTX: hipJitFallback = 0;
pub const hipJitFallback_hipJitPreferBinary: hipJitFallback = 1;
pub type hipJitFallback = ::std::os::raw::c_uint;
pub const hipLibraryOption_e_hipLibraryHostUniversalFunctionAndDataTable: hipLibraryOption_e = 0;
pub const hipLibraryOption_e_hipLibraryBinaryIsPreserved: hipLibraryOption_e = 1;
pub type hipLibraryOption_e = ::std::os::raw::c_uint;
pub use self::hipLibraryOption_e as hipLibraryOption;
pub const HIP_SUCCESS: _bindgen_ty_30 = 0;
pub const HIP_ERROR_INVALID_VALUE: _bindgen_ty_30 = 1;
pub const HIP_ERROR_NOT_INITIALIZED: _bindgen_ty_30 = 2;
pub const HIP_ERROR_LAUNCH_OUT_OF_RESOURCES: _bindgen_ty_30 = 3;
pub type _bindgen_ty_30 = ::std::os::raw::c_uint;
#[repr(C)]
#[repr(align(4))]
#[derive(Debug, Copy, Clone)]
pub struct hipDeviceArch_t {
pub _bitfield_align_1: [u8; 0],
pub _bitfield_1: __BindgenBitfieldUnit<[u8; 3usize]>,
pub __bindgen_padding_0: u8,
}
impl hipDeviceArch_t {
#[inline]
pub fn hasGlobalInt32Atomics(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(0usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasGlobalInt32Atomics(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(0usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasGlobalInt32Atomics_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
0usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasGlobalInt32Atomics_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
0usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasGlobalFloatAtomicExch(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(1usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasGlobalFloatAtomicExch(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(1usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasGlobalFloatAtomicExch_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
1usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasGlobalFloatAtomicExch_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
1usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasSharedInt32Atomics(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(2usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasSharedInt32Atomics(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(2usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasSharedInt32Atomics_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
2usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasSharedInt32Atomics_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
2usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasSharedFloatAtomicExch(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(3usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasSharedFloatAtomicExch(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(3usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasSharedFloatAtomicExch_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
3usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasSharedFloatAtomicExch_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
3usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasFloatAtomicAdd(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(4usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasFloatAtomicAdd(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(4usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasFloatAtomicAdd_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
4usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasFloatAtomicAdd_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
4usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasGlobalInt64Atomics(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(5usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasGlobalInt64Atomics(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(5usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasGlobalInt64Atomics_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
5usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasGlobalInt64Atomics_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
5usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasSharedInt64Atomics(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(6usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasSharedInt64Atomics(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(6usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasSharedInt64Atomics_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
6usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasSharedInt64Atomics_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
6usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasDoubles(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(7usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasDoubles(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(7usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasDoubles_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
7usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasDoubles_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
7usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasWarpVote(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(8usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasWarpVote(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(8usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasWarpVote_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
8usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasWarpVote_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
8usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasWarpBallot(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(9usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasWarpBallot(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(9usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasWarpBallot_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
9usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasWarpBallot_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
9usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasWarpShuffle(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(10usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasWarpShuffle(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(10usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasWarpShuffle_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
10usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasWarpShuffle_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
10usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasFunnelShift(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(11usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasFunnelShift(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(11usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasFunnelShift_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
11usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasFunnelShift_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
11usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasThreadFenceSystem(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(12usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasThreadFenceSystem(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(12usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasThreadFenceSystem_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
12usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasThreadFenceSystem_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
12usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasSyncThreadsExt(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(13usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasSyncThreadsExt(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(13usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasSyncThreadsExt_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
13usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasSyncThreadsExt_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
13usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasSurfaceFuncs(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(14usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasSurfaceFuncs(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(14usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasSurfaceFuncs_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
14usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasSurfaceFuncs_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
14usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn has3dGrid(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(15usize, 1u8) as u32) }
}
#[inline]
pub fn set_has3dGrid(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(15usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn has3dGrid_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
15usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_has3dGrid_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
15usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn hasDynamicParallelism(&self) -> ::std::os::raw::c_uint {
unsafe { ::std::mem::transmute(self._bitfield_1.get(16usize, 1u8) as u32) }
}
#[inline]
pub fn set_hasDynamicParallelism(&mut self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
self._bitfield_1.set(16usize, 1u8, val as u64)
}
}
#[inline]
pub unsafe fn hasDynamicParallelism_raw(this: *const Self) -> ::std::os::raw::c_uint {
unsafe {
::std::mem::transmute(<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_get(
::std::ptr::addr_of!((*this)._bitfield_1),
16usize,
1u8,
) as u32)
}
}
#[inline]
pub unsafe fn set_hasDynamicParallelism_raw(this: *mut Self, val: ::std::os::raw::c_uint) {
unsafe {
let val: u32 = ::std::mem::transmute(val);
<__BindgenBitfieldUnit<[u8; 3usize]>>::raw_set(
::std::ptr::addr_of_mut!((*this)._bitfield_1),
16usize,
1u8,
val as u64,
)
}
}
#[inline]
pub fn new_bitfield_1(
hasGlobalInt32Atomics: ::std::os::raw::c_uint,
hasGlobalFloatAtomicExch: ::std::os::raw::c_uint,
hasSharedInt32Atomics: ::std::os::raw::c_uint,
hasSharedFloatAtomicExch: ::std::os::raw::c_uint,
hasFloatAtomicAdd: ::std::os::raw::c_uint,
hasGlobalInt64Atomics: ::std::os::raw::c_uint,
hasSharedInt64Atomics: ::std::os::raw::c_uint,
hasDoubles: ::std::os::raw::c_uint,
hasWarpVote: ::std::os::raw::c_uint,
hasWarpBallot: ::std::os::raw::c_uint,
hasWarpShuffle: ::std::os::raw::c_uint,
hasFunnelShift: ::std::os::raw::c_uint,
hasThreadFenceSystem: ::std::os::raw::c_uint,
hasSyncThreadsExt: ::std::os::raw::c_uint,
hasSurfaceFuncs: ::std::os::raw::c_uint,
has3dGrid: ::std::os::raw::c_uint,
hasDynamicParallelism: ::std::os::raw::c_uint,
) -> __BindgenBitfieldUnit<[u8; 3usize]> {
let mut __bindgen_bitfield_unit: __BindgenBitfieldUnit<[u8; 3usize]> = Default::default();
__bindgen_bitfield_unit.set(0usize, 1u8, {
let hasGlobalInt32Atomics: u32 =
unsafe { ::std::mem::transmute(hasGlobalInt32Atomics) };
hasGlobalInt32Atomics as u64
});
__bindgen_bitfield_unit.set(1usize, 1u8, {
let hasGlobalFloatAtomicExch: u32 =
unsafe { ::std::mem::transmute(hasGlobalFloatAtomicExch) };
hasGlobalFloatAtomicExch as u64
});
__bindgen_bitfield_unit.set(2usize, 1u8, {
let hasSharedInt32Atomics: u32 =
unsafe { ::std::mem::transmute(hasSharedInt32Atomics) };
hasSharedInt32Atomics as u64
});
__bindgen_bitfield_unit.set(3usize, 1u8, {
let hasSharedFloatAtomicExch: u32 =
unsafe { ::std::mem::transmute(hasSharedFloatAtomicExch) };
hasSharedFloatAtomicExch as u64
});
__bindgen_bitfield_unit.set(4usize, 1u8, {
let hasFloatAtomicAdd: u32 = unsafe { ::std::mem::transmute(hasFloatAtomicAdd) };
hasFloatAtomicAdd as u64
});
__bindgen_bitfield_unit.set(5usize, 1u8, {
let hasGlobalInt64Atomics: u32 =
unsafe { ::std::mem::transmute(hasGlobalInt64Atomics) };
hasGlobalInt64Atomics as u64
});
__bindgen_bitfield_unit.set(6usize, 1u8, {
let hasSharedInt64Atomics: u32 =
unsafe { ::std::mem::transmute(hasSharedInt64Atomics) };
hasSharedInt64Atomics as u64
});
__bindgen_bitfield_unit.set(7usize, 1u8, {
let hasDoubles: u32 = unsafe { ::std::mem::transmute(hasDoubles) };
hasDoubles as u64
});
__bindgen_bitfield_unit.set(8usize, 1u8, {
let hasWarpVote: u32 = unsafe { ::std::mem::transmute(hasWarpVote) };
hasWarpVote as u64
});
__bindgen_bitfield_unit.set(9usize, 1u8, {
let hasWarpBallot: u32 = unsafe { ::std::mem::transmute(hasWarpBallot) };
hasWarpBallot as u64
});
__bindgen_bitfield_unit.set(10usize, 1u8, {
let hasWarpShuffle: u32 = unsafe { ::std::mem::transmute(hasWarpShuffle) };
hasWarpShuffle as u64
});
__bindgen_bitfield_unit.set(11usize, 1u8, {
let hasFunnelShift: u32 = unsafe { ::std::mem::transmute(hasFunnelShift) };
hasFunnelShift as u64
});
__bindgen_bitfield_unit.set(12usize, 1u8, {
let hasThreadFenceSystem: u32 = unsafe { ::std::mem::transmute(hasThreadFenceSystem) };
hasThreadFenceSystem as u64
});
__bindgen_bitfield_unit.set(13usize, 1u8, {
let hasSyncThreadsExt: u32 = unsafe { ::std::mem::transmute(hasSyncThreadsExt) };
hasSyncThreadsExt as u64
});
__bindgen_bitfield_unit.set(14usize, 1u8, {
let hasSurfaceFuncs: u32 = unsafe { ::std::mem::transmute(hasSurfaceFuncs) };
hasSurfaceFuncs as u64
});
__bindgen_bitfield_unit.set(15usize, 1u8, {
let has3dGrid: u32 = unsafe { ::std::mem::transmute(has3dGrid) };
has3dGrid as u64
});
__bindgen_bitfield_unit.set(16usize, 1u8, {
let hasDynamicParallelism: u32 =
unsafe { ::std::mem::transmute(hasDynamicParallelism) };
hasDynamicParallelism as u64
});
__bindgen_bitfield_unit
}
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipUUID_t {
pub bytes: [::std::os::raw::c_char; 16usize],
}
pub type hipUUID = hipUUID_t;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipDeviceProp_tR0600 {
pub name: [::std::os::raw::c_char; 256usize],
pub uuid: hipUUID,
pub luid: [::std::os::raw::c_char; 8usize],
pub luidDeviceNodeMask: ::std::os::raw::c_uint,
pub totalGlobalMem: usize,
pub sharedMemPerBlock: usize,
pub regsPerBlock: ::std::os::raw::c_int,
pub warpSize: ::std::os::raw::c_int,
pub memPitch: usize,
pub maxThreadsPerBlock: ::std::os::raw::c_int,
pub maxThreadsDim: [::std::os::raw::c_int; 3usize],
pub maxGridSize: [::std::os::raw::c_int; 3usize],
pub clockRate: ::std::os::raw::c_int,
pub totalConstMem: usize,
pub major: ::std::os::raw::c_int,
pub minor: ::std::os::raw::c_int,
pub textureAlignment: usize,
pub texturePitchAlignment: usize,
pub deviceOverlap: ::std::os::raw::c_int,
pub multiProcessorCount: ::std::os::raw::c_int,
pub kernelExecTimeoutEnabled: ::std::os::raw::c_int,
pub integrated: ::std::os::raw::c_int,
pub canMapHostMemory: ::std::os::raw::c_int,
pub computeMode: ::std::os::raw::c_int,
pub maxTexture1D: ::std::os::raw::c_int,
pub maxTexture1DMipmap: ::std::os::raw::c_int,
pub maxTexture1DLinear: ::std::os::raw::c_int,
pub maxTexture2D: [::std::os::raw::c_int; 2usize],
pub maxTexture2DMipmap: [::std::os::raw::c_int; 2usize],
pub maxTexture2DLinear: [::std::os::raw::c_int; 3usize],
pub maxTexture2DGather: [::std::os::raw::c_int; 2usize],
pub maxTexture3D: [::std::os::raw::c_int; 3usize],
pub maxTexture3DAlt: [::std::os::raw::c_int; 3usize],
pub maxTextureCubemap: ::std::os::raw::c_int,
pub maxTexture1DLayered: [::std::os::raw::c_int; 2usize],
pub maxTexture2DLayered: [::std::os::raw::c_int; 3usize],
pub maxTextureCubemapLayered: [::std::os::raw::c_int; 2usize],
pub maxSurface1D: ::std::os::raw::c_int,
pub maxSurface2D: [::std::os::raw::c_int; 2usize],
pub maxSurface3D: [::std::os::raw::c_int; 3usize],
pub maxSurface1DLayered: [::std::os::raw::c_int; 2usize],
pub maxSurface2DLayered: [::std::os::raw::c_int; 3usize],
pub maxSurfaceCubemap: ::std::os::raw::c_int,
pub maxSurfaceCubemapLayered: [::std::os::raw::c_int; 2usize],
pub surfaceAlignment: usize,
pub concurrentKernels: ::std::os::raw::c_int,
pub ECCEnabled: ::std::os::raw::c_int,
pub pciBusID: ::std::os::raw::c_int,
pub pciDeviceID: ::std::os::raw::c_int,
pub pciDomainID: ::std::os::raw::c_int,
pub tccDriver: ::std::os::raw::c_int,
pub asyncEngineCount: ::std::os::raw::c_int,
pub unifiedAddressing: ::std::os::raw::c_int,
pub memoryClockRate: ::std::os::raw::c_int,
pub memoryBusWidth: ::std::os::raw::c_int,
pub l2CacheSize: ::std::os::raw::c_int,
pub persistingL2CacheMaxSize: ::std::os::raw::c_int,
pub maxThreadsPerMultiProcessor: ::std::os::raw::c_int,
pub streamPrioritiesSupported: ::std::os::raw::c_int,
pub globalL1CacheSupported: ::std::os::raw::c_int,
pub localL1CacheSupported: ::std::os::raw::c_int,
pub sharedMemPerMultiprocessor: usize,
pub regsPerMultiprocessor: ::std::os::raw::c_int,
pub managedMemory: ::std::os::raw::c_int,
pub isMultiGpuBoard: ::std::os::raw::c_int,
pub multiGpuBoardGroupID: ::std::os::raw::c_int,
pub hostNativeAtomicSupported: ::std::os::raw::c_int,
pub singleToDoublePrecisionPerfRatio: ::std::os::raw::c_int,
pub pageableMemoryAccess: ::std::os::raw::c_int,
pub concurrentManagedAccess: ::std::os::raw::c_int,
pub computePreemptionSupported: ::std::os::raw::c_int,
pub canUseHostPointerForRegisteredMem: ::std::os::raw::c_int,
pub cooperativeLaunch: ::std::os::raw::c_int,
pub cooperativeMultiDeviceLaunch: ::std::os::raw::c_int,
pub sharedMemPerBlockOptin: usize,
pub pageableMemoryAccessUsesHostPageTables: ::std::os::raw::c_int,
pub directManagedMemAccessFromHost: ::std::os::raw::c_int,
pub maxBlocksPerMultiProcessor: ::std::os::raw::c_int,
pub accessPolicyMaxWindowSize: ::std::os::raw::c_int,
pub reservedSharedMemPerBlock: usize,
pub hostRegisterSupported: ::std::os::raw::c_int,
pub sparseHipArraySupported: ::std::os::raw::c_int,
pub hostRegisterReadOnlySupported: ::std::os::raw::c_int,
pub timelineSemaphoreInteropSupported: ::std::os::raw::c_int,
pub memoryPoolsSupported: ::std::os::raw::c_int,
pub gpuDirectRDMASupported: ::std::os::raw::c_int,
pub gpuDirectRDMAFlushWritesOptions: ::std::os::raw::c_uint,
pub gpuDirectRDMAWritesOrdering: ::std::os::raw::c_int,
pub memoryPoolSupportedHandleTypes: ::std::os::raw::c_uint,
pub deferredMappingHipArraySupported: ::std::os::raw::c_int,
pub ipcEventSupported: ::std::os::raw::c_int,
pub clusterLaunch: ::std::os::raw::c_int,
pub unifiedFunctionPointers: ::std::os::raw::c_int,
pub reserved: [::std::os::raw::c_int; 63usize],
pub hipReserved: [::std::os::raw::c_int; 32usize],
pub gcnArchName: [::std::os::raw::c_char; 256usize],
pub maxSharedMemoryPerMultiProcessor: usize,
pub clockInstructionRate: ::std::os::raw::c_int,
pub arch: hipDeviceArch_t,
pub hdpMemFlushCntl: *mut ::std::os::raw::c_uint,
pub hdpRegFlushCntl: *mut ::std::os::raw::c_uint,
pub cooperativeMultiDeviceUnmatchedFunc: ::std::os::raw::c_int,
pub cooperativeMultiDeviceUnmatchedGridDim: ::std::os::raw::c_int,
pub cooperativeMultiDeviceUnmatchedBlockDim: ::std::os::raw::c_int,
pub cooperativeMultiDeviceUnmatchedSharedMem: ::std::os::raw::c_int,
pub isLargeBar: ::std::os::raw::c_int,
pub asicRevision: ::std::os::raw::c_int,
}
pub const hipMemoryType_hipMemoryTypeUnregistered: hipMemoryType = 0;
pub const hipMemoryType_hipMemoryTypeHost: hipMemoryType = 1;
pub const hipMemoryType_hipMemoryTypeDevice: hipMemoryType = 2;
pub const hipMemoryType_hipMemoryTypeManaged: hipMemoryType = 3;
pub const hipMemoryType_hipMemoryTypeArray: hipMemoryType = 10;
pub const hipMemoryType_hipMemoryTypeUnified: hipMemoryType = 11;
pub type hipMemoryType = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipPointerAttribute_t {
pub type_: hipMemoryType,
pub device: ::std::os::raw::c_int,
pub devicePointer: *mut ::std::os::raw::c_void,
pub hostPointer: *mut ::std::os::raw::c_void,
pub isManaged: ::std::os::raw::c_int,
pub allocationFlags: ::std::os::raw::c_uint,
}
pub const hipError_t_hipSuccess: hipError_t = 0;
pub const hipError_t_hipErrorInvalidValue: hipError_t = 1;
pub const hipError_t_hipErrorOutOfMemory: hipError_t = 2;
pub const hipError_t_hipErrorMemoryAllocation: hipError_t = 2;
pub const hipError_t_hipErrorNotInitialized: hipError_t = 3;
pub const hipError_t_hipErrorInitializationError: hipError_t = 3;
pub const hipError_t_hipErrorDeinitialized: hipError_t = 4;
pub const hipError_t_hipErrorProfilerDisabled: hipError_t = 5;
pub const hipError_t_hipErrorProfilerNotInitialized: hipError_t = 6;
pub const hipError_t_hipErrorProfilerAlreadyStarted: hipError_t = 7;
pub const hipError_t_hipErrorProfilerAlreadyStopped: hipError_t = 8;
pub const hipError_t_hipErrorInvalidConfiguration: hipError_t = 9;
pub const hipError_t_hipErrorInvalidPitchValue: hipError_t = 12;
pub const hipError_t_hipErrorInvalidSymbol: hipError_t = 13;
pub const hipError_t_hipErrorInvalidDevicePointer: hipError_t = 17;
pub const hipError_t_hipErrorInvalidMemcpyDirection: hipError_t = 21;
pub const hipError_t_hipErrorInsufficientDriver: hipError_t = 35;
pub const hipError_t_hipErrorMissingConfiguration: hipError_t = 52;
pub const hipError_t_hipErrorPriorLaunchFailure: hipError_t = 53;
pub const hipError_t_hipErrorInvalidDeviceFunction: hipError_t = 98;
pub const hipError_t_hipErrorNoDevice: hipError_t = 100;
pub const hipError_t_hipErrorInvalidDevice: hipError_t = 101;
pub const hipError_t_hipErrorInvalidImage: hipError_t = 200;
pub const hipError_t_hipErrorInvalidContext: hipError_t = 201;
pub const hipError_t_hipErrorContextAlreadyCurrent: hipError_t = 202;
pub const hipError_t_hipErrorMapFailed: hipError_t = 205;
pub const hipError_t_hipErrorMapBufferObjectFailed: hipError_t = 205;
pub const hipError_t_hipErrorUnmapFailed: hipError_t = 206;
pub const hipError_t_hipErrorArrayIsMapped: hipError_t = 207;
pub const hipError_t_hipErrorAlreadyMapped: hipError_t = 208;
pub const hipError_t_hipErrorNoBinaryForGpu: hipError_t = 209;
pub const hipError_t_hipErrorAlreadyAcquired: hipError_t = 210;
pub const hipError_t_hipErrorNotMapped: hipError_t = 211;
pub const hipError_t_hipErrorNotMappedAsArray: hipError_t = 212;
pub const hipError_t_hipErrorNotMappedAsPointer: hipError_t = 213;
pub const hipError_t_hipErrorECCNotCorrectable: hipError_t = 214;
pub const hipError_t_hipErrorUnsupportedLimit: hipError_t = 215;
pub const hipError_t_hipErrorContextAlreadyInUse: hipError_t = 216;
pub const hipError_t_hipErrorPeerAccessUnsupported: hipError_t = 217;
pub const hipError_t_hipErrorInvalidKernelFile: hipError_t = 218;
pub const hipError_t_hipErrorInvalidGraphicsContext: hipError_t = 219;
pub const hipError_t_hipErrorInvalidSource: hipError_t = 300;
pub const hipError_t_hipErrorFileNotFound: hipError_t = 301;
pub const hipError_t_hipErrorSharedObjectSymbolNotFound: hipError_t = 302;
pub const hipError_t_hipErrorSharedObjectInitFailed: hipError_t = 303;
pub const hipError_t_hipErrorOperatingSystem: hipError_t = 304;
pub const hipError_t_hipErrorInvalidHandle: hipError_t = 400;
pub const hipError_t_hipErrorInvalidResourceHandle: hipError_t = 400;
pub const hipError_t_hipErrorIllegalState: hipError_t = 401;
pub const hipError_t_hipErrorNotFound: hipError_t = 500;
pub const hipError_t_hipErrorNotReady: hipError_t = 600;
pub const hipError_t_hipErrorIllegalAddress: hipError_t = 700;
pub const hipError_t_hipErrorLaunchOutOfResources: hipError_t = 701;
pub const hipError_t_hipErrorLaunchTimeOut: hipError_t = 702;
pub const hipError_t_hipErrorPeerAccessAlreadyEnabled: hipError_t = 704;
pub const hipError_t_hipErrorPeerAccessNotEnabled: hipError_t = 705;
pub const hipError_t_hipErrorSetOnActiveProcess: hipError_t = 708;
pub const hipError_t_hipErrorContextIsDestroyed: hipError_t = 709;
pub const hipError_t_hipErrorAssert: hipError_t = 710;
pub const hipError_t_hipErrorHostMemoryAlreadyRegistered: hipError_t = 712;
pub const hipError_t_hipErrorHostMemoryNotRegistered: hipError_t = 713;
pub const hipError_t_hipErrorLaunchFailure: hipError_t = 719;
pub const hipError_t_hipErrorCooperativeLaunchTooLarge: hipError_t = 720;
pub const hipError_t_hipErrorNotSupported: hipError_t = 801;
pub const hipError_t_hipErrorStreamCaptureUnsupported: hipError_t = 900;
pub const hipError_t_hipErrorStreamCaptureInvalidated: hipError_t = 901;
pub const hipError_t_hipErrorStreamCaptureMerge: hipError_t = 902;
pub const hipError_t_hipErrorStreamCaptureUnmatched: hipError_t = 903;
pub const hipError_t_hipErrorStreamCaptureUnjoined: hipError_t = 904;
pub const hipError_t_hipErrorStreamCaptureIsolation: hipError_t = 905;
pub const hipError_t_hipErrorStreamCaptureImplicit: hipError_t = 906;
pub const hipError_t_hipErrorCapturedEvent: hipError_t = 907;
pub const hipError_t_hipErrorStreamCaptureWrongThread: hipError_t = 908;
pub const hipError_t_hipErrorGraphExecUpdateFailure: hipError_t = 910;
pub const hipError_t_hipErrorInvalidChannelDescriptor: hipError_t = 911;
pub const hipError_t_hipErrorInvalidTexture: hipError_t = 912;
pub const hipError_t_hipErrorUnknown: hipError_t = 999;
pub const hipError_t_hipErrorRuntimeMemory: hipError_t = 1052;
pub const hipError_t_hipErrorRuntimeOther: hipError_t = 1053;
pub const hipError_t_hipErrorTbd: hipError_t = 1054;
pub type hipError_t = ::std::os::raw::c_uint;
pub const hipDeviceAttribute_t_hipDeviceAttributeCudaCompatibleBegin: hipDeviceAttribute_t = 0;
pub const hipDeviceAttribute_t_hipDeviceAttributeEccEnabled: hipDeviceAttribute_t = 0;
pub const hipDeviceAttribute_t_hipDeviceAttributeAccessPolicyMaxWindowSize: hipDeviceAttribute_t =
1;
pub const hipDeviceAttribute_t_hipDeviceAttributeAsyncEngineCount: hipDeviceAttribute_t = 2;
pub const hipDeviceAttribute_t_hipDeviceAttributeCanMapHostMemory: hipDeviceAttribute_t = 3;
pub const hipDeviceAttribute_t_hipDeviceAttributeCanUseHostPointerForRegisteredMem:
hipDeviceAttribute_t = 4;
pub const hipDeviceAttribute_t_hipDeviceAttributeClockRate: hipDeviceAttribute_t = 5;
pub const hipDeviceAttribute_t_hipDeviceAttributeComputeMode: hipDeviceAttribute_t = 6;
pub const hipDeviceAttribute_t_hipDeviceAttributeComputePreemptionSupported: hipDeviceAttribute_t =
7;
pub const hipDeviceAttribute_t_hipDeviceAttributeConcurrentKernels: hipDeviceAttribute_t = 8;
pub const hipDeviceAttribute_t_hipDeviceAttributeConcurrentManagedAccess: hipDeviceAttribute_t = 9;
pub const hipDeviceAttribute_t_hipDeviceAttributeCooperativeLaunch: hipDeviceAttribute_t = 10;
pub const hipDeviceAttribute_t_hipDeviceAttributeCooperativeMultiDeviceLaunch:
hipDeviceAttribute_t = 11;
pub const hipDeviceAttribute_t_hipDeviceAttributeDeviceOverlap: hipDeviceAttribute_t = 12;
pub const hipDeviceAttribute_t_hipDeviceAttributeDirectManagedMemAccessFromHost:
hipDeviceAttribute_t = 13;
pub const hipDeviceAttribute_t_hipDeviceAttributeGlobalL1CacheSupported: hipDeviceAttribute_t = 14;
pub const hipDeviceAttribute_t_hipDeviceAttributeHostNativeAtomicSupported: hipDeviceAttribute_t =
15;
pub const hipDeviceAttribute_t_hipDeviceAttributeIntegrated: hipDeviceAttribute_t = 16;
pub const hipDeviceAttribute_t_hipDeviceAttributeIsMultiGpuBoard: hipDeviceAttribute_t = 17;
pub const hipDeviceAttribute_t_hipDeviceAttributeKernelExecTimeout: hipDeviceAttribute_t = 18;
pub const hipDeviceAttribute_t_hipDeviceAttributeL2CacheSize: hipDeviceAttribute_t = 19;
pub const hipDeviceAttribute_t_hipDeviceAttributeLocalL1CacheSupported: hipDeviceAttribute_t = 20;
pub const hipDeviceAttribute_t_hipDeviceAttributeLuid: hipDeviceAttribute_t = 21;
pub const hipDeviceAttribute_t_hipDeviceAttributeLuidDeviceNodeMask: hipDeviceAttribute_t = 22;
pub const hipDeviceAttribute_t_hipDeviceAttributeComputeCapabilityMajor: hipDeviceAttribute_t = 23;
pub const hipDeviceAttribute_t_hipDeviceAttributeManagedMemory: hipDeviceAttribute_t = 24;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxBlocksPerMultiProcessor: hipDeviceAttribute_t =
25;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxBlockDimX: hipDeviceAttribute_t = 26;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxBlockDimY: hipDeviceAttribute_t = 27;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxBlockDimZ: hipDeviceAttribute_t = 28;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxGridDimX: hipDeviceAttribute_t = 29;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxGridDimY: hipDeviceAttribute_t = 30;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxGridDimZ: hipDeviceAttribute_t = 31;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxSurface1D: hipDeviceAttribute_t = 32;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxSurface1DLayered: hipDeviceAttribute_t = 33;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxSurface2D: hipDeviceAttribute_t = 34;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxSurface2DLayered: hipDeviceAttribute_t = 35;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxSurface3D: hipDeviceAttribute_t = 36;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxSurfaceCubemap: hipDeviceAttribute_t = 37;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxSurfaceCubemapLayered: hipDeviceAttribute_t =
38;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture1DWidth: hipDeviceAttribute_t = 39;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture1DLayered: hipDeviceAttribute_t = 40;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture1DLinear: hipDeviceAttribute_t = 41;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture1DMipmap: hipDeviceAttribute_t = 42;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DWidth: hipDeviceAttribute_t = 43;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DHeight: hipDeviceAttribute_t = 44;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DGather: hipDeviceAttribute_t = 45;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DLayered: hipDeviceAttribute_t = 46;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DLinear: hipDeviceAttribute_t = 47;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DMipmap: hipDeviceAttribute_t = 48;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture3DWidth: hipDeviceAttribute_t = 49;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture3DHeight: hipDeviceAttribute_t = 50;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture3DDepth: hipDeviceAttribute_t = 51;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTexture3DAlt: hipDeviceAttribute_t = 52;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTextureCubemap: hipDeviceAttribute_t = 53;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxTextureCubemapLayered: hipDeviceAttribute_t =
54;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxThreadsDim: hipDeviceAttribute_t = 55;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxThreadsPerBlock: hipDeviceAttribute_t = 56;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxThreadsPerMultiProcessor: hipDeviceAttribute_t =
57;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxPitch: hipDeviceAttribute_t = 58;
pub const hipDeviceAttribute_t_hipDeviceAttributeMemoryBusWidth: hipDeviceAttribute_t = 59;
pub const hipDeviceAttribute_t_hipDeviceAttributeMemoryClockRate: hipDeviceAttribute_t = 60;
pub const hipDeviceAttribute_t_hipDeviceAttributeComputeCapabilityMinor: hipDeviceAttribute_t = 61;
pub const hipDeviceAttribute_t_hipDeviceAttributeMultiGpuBoardGroupID: hipDeviceAttribute_t = 62;
pub const hipDeviceAttribute_t_hipDeviceAttributeMultiprocessorCount: hipDeviceAttribute_t = 63;
pub const hipDeviceAttribute_t_hipDeviceAttributeUnused1: hipDeviceAttribute_t = 64;
pub const hipDeviceAttribute_t_hipDeviceAttributePageableMemoryAccess: hipDeviceAttribute_t = 65;
pub const hipDeviceAttribute_t_hipDeviceAttributePageableMemoryAccessUsesHostPageTables:
hipDeviceAttribute_t = 66;
pub const hipDeviceAttribute_t_hipDeviceAttributePciBusId: hipDeviceAttribute_t = 67;
pub const hipDeviceAttribute_t_hipDeviceAttributePciDeviceId: hipDeviceAttribute_t = 68;
pub const hipDeviceAttribute_t_hipDeviceAttributePciDomainId: hipDeviceAttribute_t = 69;
pub const hipDeviceAttribute_t_hipDeviceAttributePciDomainID: hipDeviceAttribute_t = 69;
pub const hipDeviceAttribute_t_hipDeviceAttributePersistingL2CacheMaxSize: hipDeviceAttribute_t =
70;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxRegistersPerBlock: hipDeviceAttribute_t = 71;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxRegistersPerMultiprocessor:
hipDeviceAttribute_t = 72;
pub const hipDeviceAttribute_t_hipDeviceAttributeReservedSharedMemPerBlock: hipDeviceAttribute_t =
73;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxSharedMemoryPerBlock: hipDeviceAttribute_t = 74;
pub const hipDeviceAttribute_t_hipDeviceAttributeSharedMemPerBlockOptin: hipDeviceAttribute_t = 75;
pub const hipDeviceAttribute_t_hipDeviceAttributeSharedMemPerMultiprocessor: hipDeviceAttribute_t =
76;
pub const hipDeviceAttribute_t_hipDeviceAttributeSingleToDoublePrecisionPerfRatio:
hipDeviceAttribute_t = 77;
pub const hipDeviceAttribute_t_hipDeviceAttributeStreamPrioritiesSupported: hipDeviceAttribute_t =
78;
pub const hipDeviceAttribute_t_hipDeviceAttributeSurfaceAlignment: hipDeviceAttribute_t = 79;
pub const hipDeviceAttribute_t_hipDeviceAttributeTccDriver: hipDeviceAttribute_t = 80;
pub const hipDeviceAttribute_t_hipDeviceAttributeTextureAlignment: hipDeviceAttribute_t = 81;
pub const hipDeviceAttribute_t_hipDeviceAttributeTexturePitchAlignment: hipDeviceAttribute_t = 82;
pub const hipDeviceAttribute_t_hipDeviceAttributeTotalConstantMemory: hipDeviceAttribute_t = 83;
pub const hipDeviceAttribute_t_hipDeviceAttributeTotalGlobalMem: hipDeviceAttribute_t = 84;
pub const hipDeviceAttribute_t_hipDeviceAttributeUnifiedAddressing: hipDeviceAttribute_t = 85;
pub const hipDeviceAttribute_t_hipDeviceAttributeUnused2: hipDeviceAttribute_t = 86;
pub const hipDeviceAttribute_t_hipDeviceAttributeWarpSize: hipDeviceAttribute_t = 87;
pub const hipDeviceAttribute_t_hipDeviceAttributeMemoryPoolsSupported: hipDeviceAttribute_t = 88;
pub const hipDeviceAttribute_t_hipDeviceAttributeVirtualMemoryManagementSupported:
hipDeviceAttribute_t = 89;
pub const hipDeviceAttribute_t_hipDeviceAttributeHostRegisterSupported: hipDeviceAttribute_t = 90;
pub const hipDeviceAttribute_t_hipDeviceAttributeMemoryPoolSupportedHandleTypes:
hipDeviceAttribute_t = 91;
pub const hipDeviceAttribute_t_hipDeviceAttributeCudaCompatibleEnd: hipDeviceAttribute_t = 9999;
pub const hipDeviceAttribute_t_hipDeviceAttributeAmdSpecificBegin: hipDeviceAttribute_t = 10000;
pub const hipDeviceAttribute_t_hipDeviceAttributeClockInstructionRate: hipDeviceAttribute_t = 10000;
pub const hipDeviceAttribute_t_hipDeviceAttributeUnused3: hipDeviceAttribute_t = 10001;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxSharedMemoryPerMultiprocessor:
hipDeviceAttribute_t = 10002;
pub const hipDeviceAttribute_t_hipDeviceAttributeUnused4: hipDeviceAttribute_t = 10003;
pub const hipDeviceAttribute_t_hipDeviceAttributeUnused5: hipDeviceAttribute_t = 10004;
pub const hipDeviceAttribute_t_hipDeviceAttributeHdpMemFlushCntl: hipDeviceAttribute_t = 10005;
pub const hipDeviceAttribute_t_hipDeviceAttributeHdpRegFlushCntl: hipDeviceAttribute_t = 10006;
pub const hipDeviceAttribute_t_hipDeviceAttributeCooperativeMultiDeviceUnmatchedFunc:
hipDeviceAttribute_t = 10007;
pub const hipDeviceAttribute_t_hipDeviceAttributeCooperativeMultiDeviceUnmatchedGridDim:
hipDeviceAttribute_t = 10008;
pub const hipDeviceAttribute_t_hipDeviceAttributeCooperativeMultiDeviceUnmatchedBlockDim:
hipDeviceAttribute_t = 10009;
pub const hipDeviceAttribute_t_hipDeviceAttributeCooperativeMultiDeviceUnmatchedSharedMem:
hipDeviceAttribute_t = 10010;
pub const hipDeviceAttribute_t_hipDeviceAttributeIsLargeBar: hipDeviceAttribute_t = 10011;
pub const hipDeviceAttribute_t_hipDeviceAttributeAsicRevision: hipDeviceAttribute_t = 10012;
pub const hipDeviceAttribute_t_hipDeviceAttributeCanUseStreamWaitValue: hipDeviceAttribute_t =
10013;
pub const hipDeviceAttribute_t_hipDeviceAttributeImageSupport: hipDeviceAttribute_t = 10014;
pub const hipDeviceAttribute_t_hipDeviceAttributePhysicalMultiProcessorCount: hipDeviceAttribute_t =
10015;
pub const hipDeviceAttribute_t_hipDeviceAttributeFineGrainSupport: hipDeviceAttribute_t = 10016;
pub const hipDeviceAttribute_t_hipDeviceAttributeWallClockRate: hipDeviceAttribute_t = 10017;
pub const hipDeviceAttribute_t_hipDeviceAttributeNumberOfXccs: hipDeviceAttribute_t = 10018;
pub const hipDeviceAttribute_t_hipDeviceAttributeMaxAvailableVgprsPerThread: hipDeviceAttribute_t =
10019;
pub const hipDeviceAttribute_t_hipDeviceAttributePciChipId: hipDeviceAttribute_t = 10020;
pub const hipDeviceAttribute_t_hipDeviceAttributeAmdSpecificEnd: hipDeviceAttribute_t = 19999;
pub const hipDeviceAttribute_t_hipDeviceAttributeVendorSpecificBegin: hipDeviceAttribute_t = 20000;
pub type hipDeviceAttribute_t = ::std::os::raw::c_uint;
pub const hipDriverProcAddressQueryResult_HIP_GET_PROC_ADDRESS_SUCCESS:
hipDriverProcAddressQueryResult = 0;
pub const hipDriverProcAddressQueryResult_HIP_GET_PROC_ADDRESS_SYMBOL_NOT_FOUND:
hipDriverProcAddressQueryResult = 1;
pub const hipDriverProcAddressQueryResult_HIP_GET_PROC_ADDRESS_VERSION_NOT_SUFFICIENT:
hipDriverProcAddressQueryResult = 2;
pub type hipDriverProcAddressQueryResult = ::std::os::raw::c_uint;
pub const hipComputeMode_hipComputeModeDefault: hipComputeMode = 0;
pub const hipComputeMode_hipComputeModeExclusive: hipComputeMode = 1;
pub const hipComputeMode_hipComputeModeProhibited: hipComputeMode = 2;
pub const hipComputeMode_hipComputeModeExclusiveProcess: hipComputeMode = 3;
pub type hipComputeMode = ::std::os::raw::c_uint;
pub const hipFlushGPUDirectRDMAWritesOptions_hipFlushGPUDirectRDMAWritesOptionHost:
hipFlushGPUDirectRDMAWritesOptions = 1;
pub const hipFlushGPUDirectRDMAWritesOptions_hipFlushGPUDirectRDMAWritesOptionMemOps:
hipFlushGPUDirectRDMAWritesOptions = 2;
pub type hipFlushGPUDirectRDMAWritesOptions = ::std::os::raw::c_uint;
pub const hipGPUDirectRDMAWritesOrdering_hipGPUDirectRDMAWritesOrderingNone:
hipGPUDirectRDMAWritesOrdering = 0;
pub const hipGPUDirectRDMAWritesOrdering_hipGPUDirectRDMAWritesOrderingOwner:
hipGPUDirectRDMAWritesOrdering = 100;
pub const hipGPUDirectRDMAWritesOrdering_hipGPUDirectRDMAWritesOrderingAllDevices:
hipGPUDirectRDMAWritesOrdering = 200;
pub type hipGPUDirectRDMAWritesOrdering = ::std::os::raw::c_uint;
pub type hipDeviceptr_t = *mut ::std::os::raw::c_void;
pub const hipChannelFormatKind_hipChannelFormatKindSigned: hipChannelFormatKind = 0;
pub const hipChannelFormatKind_hipChannelFormatKindUnsigned: hipChannelFormatKind = 1;
pub const hipChannelFormatKind_hipChannelFormatKindFloat: hipChannelFormatKind = 2;
pub const hipChannelFormatKind_hipChannelFormatKindNone: hipChannelFormatKind = 3;
pub type hipChannelFormatKind = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipChannelFormatDesc {
pub x: ::std::os::raw::c_int,
pub y: ::std::os::raw::c_int,
pub z: ::std::os::raw::c_int,
pub w: ::std::os::raw::c_int,
pub f: hipChannelFormatKind,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipArray {
_unused: [u8; 0],
}
pub type hipArray_t = *mut hipArray;
pub type hipArray_const_t = *const hipArray;
pub const hipArray_Format_HIP_AD_FORMAT_UNSIGNED_INT8: hipArray_Format = 1;
pub const hipArray_Format_HIP_AD_FORMAT_UNSIGNED_INT16: hipArray_Format = 2;
pub const hipArray_Format_HIP_AD_FORMAT_UNSIGNED_INT32: hipArray_Format = 3;
pub const hipArray_Format_HIP_AD_FORMAT_SIGNED_INT8: hipArray_Format = 8;
pub const hipArray_Format_HIP_AD_FORMAT_SIGNED_INT16: hipArray_Format = 9;
pub const hipArray_Format_HIP_AD_FORMAT_SIGNED_INT32: hipArray_Format = 10;
pub const hipArray_Format_HIP_AD_FORMAT_HALF: hipArray_Format = 16;
pub const hipArray_Format_HIP_AD_FORMAT_FLOAT: hipArray_Format = 32;
pub type hipArray_Format = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_ARRAY_DESCRIPTOR {
pub Width: usize,
pub Height: usize,
pub Format: hipArray_Format,
pub NumChannels: ::std::os::raw::c_uint,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_ARRAY3D_DESCRIPTOR {
pub Width: usize,
pub Height: usize,
pub Depth: usize,
pub Format: hipArray_Format,
pub NumChannels: ::std::os::raw::c_uint,
pub Flags: ::std::os::raw::c_uint,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hip_Memcpy2D {
pub srcXInBytes: usize,
pub srcY: usize,
pub srcMemoryType: hipMemoryType,
pub srcHost: *const ::std::os::raw::c_void,
pub srcDevice: hipDeviceptr_t,
pub srcArray: hipArray_t,
pub srcPitch: usize,
pub dstXInBytes: usize,
pub dstY: usize,
pub dstMemoryType: hipMemoryType,
pub dstHost: *mut ::std::os::raw::c_void,
pub dstDevice: hipDeviceptr_t,
pub dstArray: hipArray_t,
pub dstPitch: usize,
pub WidthInBytes: usize,
pub Height: usize,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMipmappedArray {
pub data: *mut ::std::os::raw::c_void,
pub desc: hipChannelFormatDesc,
pub type_: ::std::os::raw::c_uint,
pub width: ::std::os::raw::c_uint,
pub height: ::std::os::raw::c_uint,
pub depth: ::std::os::raw::c_uint,
pub min_mipmap_level: ::std::os::raw::c_uint,
pub max_mipmap_level: ::std::os::raw::c_uint,
pub flags: ::std::os::raw::c_uint,
pub format: hipArray_Format,
pub num_channels: ::std::os::raw::c_uint,
}
pub type hipMipmappedArray_t = *mut hipMipmappedArray;
pub type hipmipmappedArray = hipMipmappedArray_t;
pub type hipMipmappedArray_const_t = *const hipMipmappedArray;
pub const hipResourceType_hipResourceTypeArray: hipResourceType = 0;
pub const hipResourceType_hipResourceTypeMipmappedArray: hipResourceType = 1;
pub const hipResourceType_hipResourceTypeLinear: hipResourceType = 2;
pub const hipResourceType_hipResourceTypePitch2D: hipResourceType = 3;
pub type hipResourceType = ::std::os::raw::c_uint;
pub const HIPresourcetype_enum_HIP_RESOURCE_TYPE_ARRAY: HIPresourcetype_enum = 0;
pub const HIPresourcetype_enum_HIP_RESOURCE_TYPE_MIPMAPPED_ARRAY: HIPresourcetype_enum = 1;
pub const HIPresourcetype_enum_HIP_RESOURCE_TYPE_LINEAR: HIPresourcetype_enum = 2;
pub const HIPresourcetype_enum_HIP_RESOURCE_TYPE_PITCH2D: HIPresourcetype_enum = 3;
pub type HIPresourcetype_enum = ::std::os::raw::c_uint;
pub use self::HIPresourcetype_enum as HIPresourcetype;
pub use self::HIPresourcetype_enum as hipResourcetype;
pub const HIPaddress_mode_enum_HIP_TR_ADDRESS_MODE_WRAP: HIPaddress_mode_enum = 0;
pub const HIPaddress_mode_enum_HIP_TR_ADDRESS_MODE_CLAMP: HIPaddress_mode_enum = 1;
pub const HIPaddress_mode_enum_HIP_TR_ADDRESS_MODE_MIRROR: HIPaddress_mode_enum = 2;
pub const HIPaddress_mode_enum_HIP_TR_ADDRESS_MODE_BORDER: HIPaddress_mode_enum = 3;
pub type HIPaddress_mode_enum = ::std::os::raw::c_uint;
pub use self::HIPaddress_mode_enum as HIPaddress_mode;
pub const HIPfilter_mode_enum_HIP_TR_FILTER_MODE_POINT: HIPfilter_mode_enum = 0;
pub const HIPfilter_mode_enum_HIP_TR_FILTER_MODE_LINEAR: HIPfilter_mode_enum = 1;
pub type HIPfilter_mode_enum = ::std::os::raw::c_uint;
pub use self::HIPfilter_mode_enum as HIPfilter_mode;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_TEXTURE_DESC_st {
pub addressMode: [HIPaddress_mode; 3usize],
pub filterMode: HIPfilter_mode,
pub flags: ::std::os::raw::c_uint,
pub maxAnisotropy: ::std::os::raw::c_uint,
pub mipmapFilterMode: HIPfilter_mode,
pub mipmapLevelBias: f32,
pub minMipmapLevelClamp: f32,
pub maxMipmapLevelClamp: f32,
pub borderColor: [f32; 4usize],
pub reserved: [::std::os::raw::c_int; 12usize],
}
pub type HIP_TEXTURE_DESC = HIP_TEXTURE_DESC_st;
pub const hipResourceViewFormat_hipResViewFormatNone: hipResourceViewFormat = 0;
pub const hipResourceViewFormat_hipResViewFormatUnsignedChar1: hipResourceViewFormat = 1;
pub const hipResourceViewFormat_hipResViewFormatUnsignedChar2: hipResourceViewFormat = 2;
pub const hipResourceViewFormat_hipResViewFormatUnsignedChar4: hipResourceViewFormat = 3;
pub const hipResourceViewFormat_hipResViewFormatSignedChar1: hipResourceViewFormat = 4;
pub const hipResourceViewFormat_hipResViewFormatSignedChar2: hipResourceViewFormat = 5;
pub const hipResourceViewFormat_hipResViewFormatSignedChar4: hipResourceViewFormat = 6;
pub const hipResourceViewFormat_hipResViewFormatUnsignedShort1: hipResourceViewFormat = 7;
pub const hipResourceViewFormat_hipResViewFormatUnsignedShort2: hipResourceViewFormat = 8;
pub const hipResourceViewFormat_hipResViewFormatUnsignedShort4: hipResourceViewFormat = 9;
pub const hipResourceViewFormat_hipResViewFormatSignedShort1: hipResourceViewFormat = 10;
pub const hipResourceViewFormat_hipResViewFormatSignedShort2: hipResourceViewFormat = 11;
pub const hipResourceViewFormat_hipResViewFormatSignedShort4: hipResourceViewFormat = 12;
pub const hipResourceViewFormat_hipResViewFormatUnsignedInt1: hipResourceViewFormat = 13;
pub const hipResourceViewFormat_hipResViewFormatUnsignedInt2: hipResourceViewFormat = 14;
pub const hipResourceViewFormat_hipResViewFormatUnsignedInt4: hipResourceViewFormat = 15;
pub const hipResourceViewFormat_hipResViewFormatSignedInt1: hipResourceViewFormat = 16;
pub const hipResourceViewFormat_hipResViewFormatSignedInt2: hipResourceViewFormat = 17;
pub const hipResourceViewFormat_hipResViewFormatSignedInt4: hipResourceViewFormat = 18;
pub const hipResourceViewFormat_hipResViewFormatHalf1: hipResourceViewFormat = 19;
pub const hipResourceViewFormat_hipResViewFormatHalf2: hipResourceViewFormat = 20;
pub const hipResourceViewFormat_hipResViewFormatHalf4: hipResourceViewFormat = 21;
pub const hipResourceViewFormat_hipResViewFormatFloat1: hipResourceViewFormat = 22;
pub const hipResourceViewFormat_hipResViewFormatFloat2: hipResourceViewFormat = 23;
pub const hipResourceViewFormat_hipResViewFormatFloat4: hipResourceViewFormat = 24;
pub const hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed1: hipResourceViewFormat =
25;
pub const hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed2: hipResourceViewFormat =
26;
pub const hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed3: hipResourceViewFormat =
27;
pub const hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed4: hipResourceViewFormat =
28;
pub const hipResourceViewFormat_hipResViewFormatSignedBlockCompressed4: hipResourceViewFormat = 29;
pub const hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed5: hipResourceViewFormat =
30;
pub const hipResourceViewFormat_hipResViewFormatSignedBlockCompressed5: hipResourceViewFormat = 31;
pub const hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed6H: hipResourceViewFormat =
32;
pub const hipResourceViewFormat_hipResViewFormatSignedBlockCompressed6H: hipResourceViewFormat = 33;
pub const hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed7: hipResourceViewFormat =
34;
pub type hipResourceViewFormat = ::std::os::raw::c_uint;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_NONE: HIPresourceViewFormat_enum = 0;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_1X8: HIPresourceViewFormat_enum = 1;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_2X8: HIPresourceViewFormat_enum = 2;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_4X8: HIPresourceViewFormat_enum = 3;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_1X8: HIPresourceViewFormat_enum = 4;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_2X8: HIPresourceViewFormat_enum = 5;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_4X8: HIPresourceViewFormat_enum = 6;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_1X16: HIPresourceViewFormat_enum = 7;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_2X16: HIPresourceViewFormat_enum = 8;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_4X16: HIPresourceViewFormat_enum = 9;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_1X16: HIPresourceViewFormat_enum = 10;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_2X16: HIPresourceViewFormat_enum = 11;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_4X16: HIPresourceViewFormat_enum = 12;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_1X32: HIPresourceViewFormat_enum = 13;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_2X32: HIPresourceViewFormat_enum = 14;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_4X32: HIPresourceViewFormat_enum = 15;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_1X32: HIPresourceViewFormat_enum = 16;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_2X32: HIPresourceViewFormat_enum = 17;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_4X32: HIPresourceViewFormat_enum = 18;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_1X16: HIPresourceViewFormat_enum =
19;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_2X16: HIPresourceViewFormat_enum =
20;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_4X16: HIPresourceViewFormat_enum =
21;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_1X32: HIPresourceViewFormat_enum =
22;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_2X32: HIPresourceViewFormat_enum =
23;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_4X32: HIPresourceViewFormat_enum =
24;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC1: HIPresourceViewFormat_enum =
25;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC2: HIPresourceViewFormat_enum =
26;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC3: HIPresourceViewFormat_enum =
27;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC4: HIPresourceViewFormat_enum =
28;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SIGNED_BC4: HIPresourceViewFormat_enum =
29;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC5: HIPresourceViewFormat_enum =
30;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SIGNED_BC5: HIPresourceViewFormat_enum =
31;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC6H: HIPresourceViewFormat_enum =
32;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SIGNED_BC6H: HIPresourceViewFormat_enum =
33;
pub const HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC7: HIPresourceViewFormat_enum =
34;
pub type HIPresourceViewFormat_enum = ::std::os::raw::c_uint;
pub use self::HIPresourceViewFormat_enum as HIPresourceViewFormat;
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipResourceDesc {
pub resType: hipResourceType,
pub res: hipResourceDesc__bindgen_ty_1,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipResourceDesc__bindgen_ty_1 {
pub array: hipResourceDesc__bindgen_ty_1__bindgen_ty_1,
pub mipmap: hipResourceDesc__bindgen_ty_1__bindgen_ty_2,
pub linear: hipResourceDesc__bindgen_ty_1__bindgen_ty_3,
pub pitch2D: hipResourceDesc__bindgen_ty_1__bindgen_ty_4,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipResourceDesc__bindgen_ty_1__bindgen_ty_1 {
pub array: hipArray_t,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipResourceDesc__bindgen_ty_1__bindgen_ty_2 {
pub mipmap: hipMipmappedArray_t,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipResourceDesc__bindgen_ty_1__bindgen_ty_3 {
pub devPtr: *mut ::std::os::raw::c_void,
pub desc: hipChannelFormatDesc,
pub sizeInBytes: usize,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipResourceDesc__bindgen_ty_1__bindgen_ty_4 {
pub devPtr: *mut ::std::os::raw::c_void,
pub desc: hipChannelFormatDesc,
pub width: usize,
pub height: usize,
pub pitchInBytes: usize,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub struct HIP_RESOURCE_DESC_st {
pub resType: HIPresourcetype,
pub res: HIP_RESOURCE_DESC_st__bindgen_ty_1,
pub flags: ::std::os::raw::c_uint,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union HIP_RESOURCE_DESC_st__bindgen_ty_1 {
pub array: HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_1,
pub mipmap: HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_2,
pub linear: HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_3,
pub pitch2D: HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_4,
pub reserved: HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_5,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_1 {
pub hArray: hipArray_t,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_2 {
pub hMipmappedArray: hipMipmappedArray_t,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_3 {
pub devPtr: hipDeviceptr_t,
pub format: hipArray_Format,
pub numChannels: ::std::os::raw::c_uint,
pub sizeInBytes: usize,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_4 {
pub devPtr: hipDeviceptr_t,
pub format: hipArray_Format,
pub numChannels: ::std::os::raw::c_uint,
pub width: usize,
pub height: usize,
pub pitchInBytes: usize,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_5 {
pub reserved: [::std::os::raw::c_int; 32usize],
}
pub type HIP_RESOURCE_DESC = HIP_RESOURCE_DESC_st;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipResourceViewDesc {
pub format: hipResourceViewFormat,
pub width: usize,
pub height: usize,
pub depth: usize,
pub firstMipmapLevel: ::std::os::raw::c_uint,
pub lastMipmapLevel: ::std::os::raw::c_uint,
pub firstLayer: ::std::os::raw::c_uint,
pub lastLayer: ::std::os::raw::c_uint,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_RESOURCE_VIEW_DESC_st {
pub format: HIPresourceViewFormat,
pub width: usize,
pub height: usize,
pub depth: usize,
pub firstMipmapLevel: ::std::os::raw::c_uint,
pub lastMipmapLevel: ::std::os::raw::c_uint,
pub firstLayer: ::std::os::raw::c_uint,
pub lastLayer: ::std::os::raw::c_uint,
pub reserved: [::std::os::raw::c_uint; 16usize],
}
pub type HIP_RESOURCE_VIEW_DESC = HIP_RESOURCE_VIEW_DESC_st;
pub const hipMemcpyKind_hipMemcpyHostToHost: hipMemcpyKind = 0;
pub const hipMemcpyKind_hipMemcpyHostToDevice: hipMemcpyKind = 1;
pub const hipMemcpyKind_hipMemcpyDeviceToHost: hipMemcpyKind = 2;
pub const hipMemcpyKind_hipMemcpyDeviceToDevice: hipMemcpyKind = 3;
pub const hipMemcpyKind_hipMemcpyDefault: hipMemcpyKind = 4;
pub const hipMemcpyKind_hipMemcpyDeviceToDeviceNoCU: hipMemcpyKind = 1024;
pub type hipMemcpyKind = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipPitchedPtr {
pub ptr: *mut ::std::os::raw::c_void,
pub pitch: usize,
pub xsize: usize,
pub ysize: usize,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExtent {
pub width: usize,
pub height: usize,
pub depth: usize,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipPos {
pub x: usize,
pub y: usize,
pub z: usize,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemcpy3DParms {
pub srcArray: hipArray_t,
pub srcPos: hipPos,
pub srcPtr: hipPitchedPtr,
pub dstArray: hipArray_t,
pub dstPos: hipPos,
pub dstPtr: hipPitchedPtr,
pub extent: hipExtent,
pub kind: hipMemcpyKind,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_MEMCPY3D {
pub srcXInBytes: usize,
pub srcY: usize,
pub srcZ: usize,
pub srcLOD: usize,
pub srcMemoryType: hipMemoryType,
pub srcHost: *const ::std::os::raw::c_void,
pub srcDevice: hipDeviceptr_t,
pub srcArray: hipArray_t,
pub srcPitch: usize,
pub srcHeight: usize,
pub dstXInBytes: usize,
pub dstY: usize,
pub dstZ: usize,
pub dstLOD: usize,
pub dstMemoryType: hipMemoryType,
pub dstHost: *mut ::std::os::raw::c_void,
pub dstDevice: hipDeviceptr_t,
pub dstArray: hipArray_t,
pub dstPitch: usize,
pub dstHeight: usize,
pub WidthInBytes: usize,
pub Height: usize,
pub Depth: usize,
}
pub const hipMemLocationType_hipMemLocationTypeInvalid: hipMemLocationType = 0;
pub const hipMemLocationType_hipMemLocationTypeNone: hipMemLocationType = 0;
pub const hipMemLocationType_hipMemLocationTypeDevice: hipMemLocationType = 1;
pub const hipMemLocationType_hipMemLocationTypeHost: hipMemLocationType = 2;
pub const hipMemLocationType_hipMemLocationTypeHostNuma: hipMemLocationType = 3;
pub const hipMemLocationType_hipMemLocationTypeHostNumaCurrent: hipMemLocationType = 4;
pub type hipMemLocationType = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemLocation {
pub type_: hipMemLocationType,
pub id: ::std::os::raw::c_int,
}
pub const hipMemcpyFlags_hipMemcpyFlagDefault: hipMemcpyFlags = 0;
pub const hipMemcpyFlags_hipMemcpyFlagPreferOverlapWithCompute: hipMemcpyFlags = 1;
pub type hipMemcpyFlags = ::std::os::raw::c_uint;
pub const hipMemcpySrcAccessOrder_hipMemcpySrcAccessOrderInvalid: hipMemcpySrcAccessOrder = 0;
pub const hipMemcpySrcAccessOrder_hipMemcpySrcAccessOrderStream: hipMemcpySrcAccessOrder = 1;
pub const hipMemcpySrcAccessOrder_hipMemcpySrcAccessOrderDuringApiCall: hipMemcpySrcAccessOrder = 2;
pub const hipMemcpySrcAccessOrder_hipMemcpySrcAccessOrderAny: hipMemcpySrcAccessOrder = 3;
pub const hipMemcpySrcAccessOrder_hipMemcpySrcAccessOrderMax: hipMemcpySrcAccessOrder = 2147483647;
pub type hipMemcpySrcAccessOrder = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemcpyAttributes {
pub srcAccessOrder: hipMemcpySrcAccessOrder,
pub srcLocHint: hipMemLocation,
pub dstLocHint: hipMemLocation,
pub flags: ::std::os::raw::c_uint,
}
pub const hipMemcpy3DOperandType_hipMemcpyOperandTypePointer: hipMemcpy3DOperandType = 1;
pub const hipMemcpy3DOperandType_hipMemcpyOperandTypeArray: hipMemcpy3DOperandType = 2;
pub const hipMemcpy3DOperandType_hipMemcpyOperandTypeMax: hipMemcpy3DOperandType = 2147483647;
pub type hipMemcpy3DOperandType = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipOffset3D {
pub x: usize,
pub y: usize,
pub z: usize,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipMemcpy3DOperand {
pub type_: hipMemcpy3DOperandType,
pub op: hipMemcpy3DOperand__bindgen_ty_1,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipMemcpy3DOperand__bindgen_ty_1 {
pub ptr: hipMemcpy3DOperand__bindgen_ty_1__bindgen_ty_1,
pub array: hipMemcpy3DOperand__bindgen_ty_1__bindgen_ty_2,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemcpy3DOperand__bindgen_ty_1__bindgen_ty_1 {
pub ptr: *mut ::std::os::raw::c_void,
pub rowLength: usize,
pub layerHeight: usize,
pub locHint: hipMemLocation,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemcpy3DOperand__bindgen_ty_1__bindgen_ty_2 {
pub array: hipArray_t,
pub offset: hipOffset3D,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipMemcpy3DBatchOp {
pub src: hipMemcpy3DOperand,
pub dst: hipMemcpy3DOperand,
pub extent: hipExtent,
pub srcAccessOrder: hipMemcpySrcAccessOrder,
pub flags: ::std::os::raw::c_uint,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemcpy3DPeerParms {
pub srcArray: hipArray_t,
pub srcPos: hipPos,
pub srcPtr: hipPitchedPtr,
pub srcDevice: ::std::os::raw::c_int,
pub dstArray: hipArray_t,
pub dstPos: hipPos,
pub dstPtr: hipPitchedPtr,
pub dstDevice: ::std::os::raw::c_int,
pub extent: hipExtent,
}
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_MAX_THREADS_PER_BLOCK: hipFunction_attribute = 0;
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_SHARED_SIZE_BYTES: hipFunction_attribute = 1;
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_CONST_SIZE_BYTES: hipFunction_attribute = 2;
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_LOCAL_SIZE_BYTES: hipFunction_attribute = 3;
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_NUM_REGS: hipFunction_attribute = 4;
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_PTX_VERSION: hipFunction_attribute = 5;
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_BINARY_VERSION: hipFunction_attribute = 6;
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_CACHE_MODE_CA: hipFunction_attribute = 7;
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_MAX_DYNAMIC_SHARED_SIZE_BYTES:
hipFunction_attribute = 8;
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_PREFERRED_SHARED_MEMORY_CARVEOUT:
hipFunction_attribute = 9;
pub const hipFunction_attribute_HIP_FUNC_ATTRIBUTE_MAX: hipFunction_attribute = 10;
pub type hipFunction_attribute = ::std::os::raw::c_uint;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_CONTEXT: hipPointer_attribute = 1;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_MEMORY_TYPE: hipPointer_attribute = 2;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_DEVICE_POINTER: hipPointer_attribute = 3;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_HOST_POINTER: hipPointer_attribute = 4;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_P2P_TOKENS: hipPointer_attribute = 5;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_SYNC_MEMOPS: hipPointer_attribute = 6;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_BUFFER_ID: hipPointer_attribute = 7;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_IS_MANAGED: hipPointer_attribute = 8;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_DEVICE_ORDINAL: hipPointer_attribute = 9;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_IS_LEGACY_HIP_IPC_CAPABLE:
hipPointer_attribute = 10;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_RANGE_START_ADDR: hipPointer_attribute = 11;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_RANGE_SIZE: hipPointer_attribute = 12;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_MAPPED: hipPointer_attribute = 13;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_ALLOWED_HANDLE_TYPES: hipPointer_attribute =
14;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_IS_GPU_DIRECT_RDMA_CAPABLE:
hipPointer_attribute = 15;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_ACCESS_FLAGS: hipPointer_attribute = 16;
pub const hipPointer_attribute_HIP_POINTER_ATTRIBUTE_MEMPOOL_HANDLE: hipPointer_attribute = 17;
pub type hipPointer_attribute = ::std::os::raw::c_uint;
unsafe extern "C" {
#[link_name = "\u{1}_ZN8hip_impl8hip_initEv"]
pub fn hip_impl_hip_init() -> hipError_t;
}
unsafe extern "C" {
pub fn hipCreateChannelDesc(
x: ::std::os::raw::c_int,
y: ::std::os::raw::c_int,
z: ::std::os::raw::c_int,
w: ::std::os::raw::c_int,
f: hipChannelFormatKind,
) -> hipChannelFormatDesc;
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct __hip_texture {
_unused: [u8; 0],
}
pub type hipTextureObject_t = *mut __hip_texture;
pub const hipTextureAddressMode_hipAddressModeWrap: hipTextureAddressMode = 0;
pub const hipTextureAddressMode_hipAddressModeClamp: hipTextureAddressMode = 1;
pub const hipTextureAddressMode_hipAddressModeMirror: hipTextureAddressMode = 2;
pub const hipTextureAddressMode_hipAddressModeBorder: hipTextureAddressMode = 3;
pub type hipTextureAddressMode = ::std::os::raw::c_uint;
pub const hipTextureFilterMode_hipFilterModePoint: hipTextureFilterMode = 0;
pub const hipTextureFilterMode_hipFilterModeLinear: hipTextureFilterMode = 1;
pub type hipTextureFilterMode = ::std::os::raw::c_uint;
pub const hipTextureReadMode_hipReadModeElementType: hipTextureReadMode = 0;
pub const hipTextureReadMode_hipReadModeNormalizedFloat: hipTextureReadMode = 1;
pub type hipTextureReadMode = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct textureReference {
pub normalized: ::std::os::raw::c_int,
pub readMode: hipTextureReadMode,
pub filterMode: hipTextureFilterMode,
pub addressMode: [hipTextureAddressMode; 3usize],
pub channelDesc: hipChannelFormatDesc,
pub sRGB: ::std::os::raw::c_int,
pub maxAnisotropy: ::std::os::raw::c_uint,
pub mipmapFilterMode: hipTextureFilterMode,
pub mipmapLevelBias: f32,
pub minMipmapLevelClamp: f32,
pub maxMipmapLevelClamp: f32,
pub textureObject: hipTextureObject_t,
pub numChannels: ::std::os::raw::c_int,
pub format: hipArray_Format,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipTextureDesc {
pub addressMode: [hipTextureAddressMode; 3usize],
pub filterMode: hipTextureFilterMode,
pub readMode: hipTextureReadMode,
pub sRGB: ::std::os::raw::c_int,
pub borderColor: [f32; 4usize],
pub normalizedCoords: ::std::os::raw::c_int,
pub maxAnisotropy: ::std::os::raw::c_uint,
pub mipmapFilterMode: hipTextureFilterMode,
pub mipmapLevelBias: f32,
pub minMipmapLevelClamp: f32,
pub maxMipmapLevelClamp: f32,
}
pub type hipTexRef = *mut textureReference;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct __hip_surface {
_unused: [u8; 0],
}
pub type hipSurfaceObject_t = *mut __hip_surface;
pub const hipSurfaceBoundaryMode_hipBoundaryModeZero: hipSurfaceBoundaryMode = 0;
pub const hipSurfaceBoundaryMode_hipBoundaryModeTrap: hipSurfaceBoundaryMode = 1;
pub const hipSurfaceBoundaryMode_hipBoundaryModeClamp: hipSurfaceBoundaryMode = 2;
pub type hipSurfaceBoundaryMode = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipCtx_t {
_unused: [u8; 0],
}
pub type hipCtx_t = *mut ihipCtx_t;
pub type hipDevice_t = ::std::os::raw::c_int;
pub const hipDeviceP2PAttr_hipDevP2PAttrPerformanceRank: hipDeviceP2PAttr = 0;
pub const hipDeviceP2PAttr_hipDevP2PAttrAccessSupported: hipDeviceP2PAttr = 1;
pub const hipDeviceP2PAttr_hipDevP2PAttrNativeAtomicSupported: hipDeviceP2PAttr = 2;
pub const hipDeviceP2PAttr_hipDevP2PAttrHipArrayAccessSupported: hipDeviceP2PAttr = 3;
pub type hipDeviceP2PAttr = ::std::os::raw::c_uint;
pub const hipDriverEntryPointQueryResult_hipDriverEntryPointSuccess:
hipDriverEntryPointQueryResult = 0;
pub const hipDriverEntryPointQueryResult_hipDriverEntryPointSymbolNotFound:
hipDriverEntryPointQueryResult = 1;
pub const hipDriverEntryPointQueryResult_hipDriverEntryPointVersionNotSufficent:
hipDriverEntryPointQueryResult = 2;
pub type hipDriverEntryPointQueryResult = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipStream_t {
_unused: [u8; 0],
}
pub type hipStream_t = *mut ihipStream_t;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipIpcMemHandle_st {
pub reserved: [::std::os::raw::c_char; 64usize],
}
pub type hipIpcMemHandle_t = hipIpcMemHandle_st;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipIpcEventHandle_st {
pub reserved: [::std::os::raw::c_char; 64usize],
}
pub type hipIpcEventHandle_t = hipIpcEventHandle_st;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipModule_t {
_unused: [u8; 0],
}
pub type hipModule_t = *mut ihipModule_t;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipModuleSymbol_t {
_unused: [u8; 0],
}
pub type hipFunction_t = *mut ihipModuleSymbol_t;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipLinkState_t {
_unused: [u8; 0],
}
pub type hipLinkState_t = *mut ihipLinkState_t;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipLibrary_t {
_unused: [u8; 0],
}
pub type hipLibrary_t = *mut ihipLibrary_t;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipKernel_t {
_unused: [u8; 0],
}
pub type hipKernel_t = *mut ihipKernel_t;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipMemPoolHandle_t {
_unused: [u8; 0],
}
pub type hipMemPool_t = *mut ihipMemPoolHandle_t;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipFuncAttributes {
pub binaryVersion: ::std::os::raw::c_int,
pub cacheModeCA: ::std::os::raw::c_int,
pub constSizeBytes: usize,
pub localSizeBytes: usize,
pub maxDynamicSharedSizeBytes: ::std::os::raw::c_int,
pub maxThreadsPerBlock: ::std::os::raw::c_int,
pub numRegs: ::std::os::raw::c_int,
pub preferredShmemCarveout: ::std::os::raw::c_int,
pub ptxVersion: ::std::os::raw::c_int,
pub sharedSizeBytes: usize,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipEvent_t {
_unused: [u8; 0],
}
pub type hipEvent_t = *mut ihipEvent_t;
pub const hipLimit_t_hipLimitStackSize: hipLimit_t = 0;
pub const hipLimit_t_hipLimitPrintfFifoSize: hipLimit_t = 1;
pub const hipLimit_t_hipLimitMallocHeapSize: hipLimit_t = 2;
pub const hipLimit_t_hipExtLimitScratchMin: hipLimit_t = 4096;
pub const hipLimit_t_hipExtLimitScratchMax: hipLimit_t = 4097;
pub const hipLimit_t_hipExtLimitScratchCurrent: hipLimit_t = 4098;
pub const hipLimit_t_hipLimitRange: hipLimit_t = 4099;
pub type hipLimit_t = ::std::os::raw::c_uint;
pub const hipStreamBatchMemOpType_hipStreamMemOpWaitValue32: hipStreamBatchMemOpType = 1;
pub const hipStreamBatchMemOpType_hipStreamMemOpWriteValue32: hipStreamBatchMemOpType = 2;
pub const hipStreamBatchMemOpType_hipStreamMemOpWaitValue64: hipStreamBatchMemOpType = 4;
pub const hipStreamBatchMemOpType_hipStreamMemOpWriteValue64: hipStreamBatchMemOpType = 5;
pub const hipStreamBatchMemOpType_hipStreamMemOpBarrier: hipStreamBatchMemOpType = 6;
pub const hipStreamBatchMemOpType_hipStreamMemOpFlushRemoteWrites: hipStreamBatchMemOpType = 3;
pub type hipStreamBatchMemOpType = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipStreamBatchMemOpParams_union {
pub operation: hipStreamBatchMemOpType,
pub waitValue: hipStreamBatchMemOpParams_union_hipStreamMemOpWaitValueParams_t,
pub writeValue: hipStreamBatchMemOpParams_union_hipStreamMemOpWriteValueParams_t,
pub flushRemoteWrites: hipStreamBatchMemOpParams_union_hipStreamMemOpFlushRemoteWritesParams_t,
pub memoryBarrier: hipStreamBatchMemOpParams_union_hipStreamMemOpMemoryBarrierParams_t,
pub pad: [u64; 6usize],
}
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipStreamBatchMemOpParams_union_hipStreamMemOpWaitValueParams_t {
pub operation: hipStreamBatchMemOpType,
pub address: hipDeviceptr_t,
pub __bindgen_anon_1:
hipStreamBatchMemOpParams_union_hipStreamMemOpWaitValueParams_t__bindgen_ty_1,
pub flags: ::std::os::raw::c_uint,
pub alias: hipDeviceptr_t,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipStreamBatchMemOpParams_union_hipStreamMemOpWaitValueParams_t__bindgen_ty_1 {
pub value: u32,
pub value64: u64,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipStreamBatchMemOpParams_union_hipStreamMemOpWriteValueParams_t {
pub operation: hipStreamBatchMemOpType,
pub address: hipDeviceptr_t,
pub __bindgen_anon_1:
hipStreamBatchMemOpParams_union_hipStreamMemOpWriteValueParams_t__bindgen_ty_1,
pub flags: ::std::os::raw::c_uint,
pub alias: hipDeviceptr_t,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipStreamBatchMemOpParams_union_hipStreamMemOpWriteValueParams_t__bindgen_ty_1 {
pub value: u32,
pub value64: u64,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipStreamBatchMemOpParams_union_hipStreamMemOpFlushRemoteWritesParams_t {
pub operation: hipStreamBatchMemOpType,
pub flags: ::std::os::raw::c_uint,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipStreamBatchMemOpParams_union_hipStreamMemOpMemoryBarrierParams_t {
pub operation: hipStreamBatchMemOpType,
pub flags: ::std::os::raw::c_uint,
}
pub type hipStreamBatchMemOpParams = hipStreamBatchMemOpParams_union;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipBatchMemOpNodeParams {
pub ctx: hipCtx_t,
pub count: ::std::os::raw::c_uint,
pub paramArray: *mut hipStreamBatchMemOpParams,
pub flags: ::std::os::raw::c_uint,
}
pub const hipMemoryAdvise_hipMemAdviseSetReadMostly: hipMemoryAdvise = 1;
pub const hipMemoryAdvise_hipMemAdviseUnsetReadMostly: hipMemoryAdvise = 2;
pub const hipMemoryAdvise_hipMemAdviseSetPreferredLocation: hipMemoryAdvise = 3;
pub const hipMemoryAdvise_hipMemAdviseUnsetPreferredLocation: hipMemoryAdvise = 4;
pub const hipMemoryAdvise_hipMemAdviseSetAccessedBy: hipMemoryAdvise = 5;
pub const hipMemoryAdvise_hipMemAdviseUnsetAccessedBy: hipMemoryAdvise = 6;
pub const hipMemoryAdvise_hipMemAdviseSetCoarseGrain: hipMemoryAdvise = 100;
pub const hipMemoryAdvise_hipMemAdviseUnsetCoarseGrain: hipMemoryAdvise = 101;
pub type hipMemoryAdvise = ::std::os::raw::c_uint;
pub const hipMemRangeCoherencyMode_hipMemRangeCoherencyModeFineGrain: hipMemRangeCoherencyMode = 0;
pub const hipMemRangeCoherencyMode_hipMemRangeCoherencyModeCoarseGrain: hipMemRangeCoherencyMode =
1;
pub const hipMemRangeCoherencyMode_hipMemRangeCoherencyModeIndeterminate: hipMemRangeCoherencyMode =
2;
pub type hipMemRangeCoherencyMode = ::std::os::raw::c_uint;
pub const hipMemRangeAttribute_hipMemRangeAttributeReadMostly: hipMemRangeAttribute = 1;
pub const hipMemRangeAttribute_hipMemRangeAttributePreferredLocation: hipMemRangeAttribute = 2;
pub const hipMemRangeAttribute_hipMemRangeAttributeAccessedBy: hipMemRangeAttribute = 3;
pub const hipMemRangeAttribute_hipMemRangeAttributeLastPrefetchLocation: hipMemRangeAttribute = 4;
pub const hipMemRangeAttribute_hipMemRangeAttributeCoherencyMode: hipMemRangeAttribute = 100;
pub type hipMemRangeAttribute = ::std::os::raw::c_uint;
pub const hipMemPoolAttr_hipMemPoolReuseFollowEventDependencies: hipMemPoolAttr = 1;
pub const hipMemPoolAttr_hipMemPoolReuseAllowOpportunistic: hipMemPoolAttr = 2;
pub const hipMemPoolAttr_hipMemPoolReuseAllowInternalDependencies: hipMemPoolAttr = 3;
pub const hipMemPoolAttr_hipMemPoolAttrReleaseThreshold: hipMemPoolAttr = 4;
pub const hipMemPoolAttr_hipMemPoolAttrReservedMemCurrent: hipMemPoolAttr = 5;
pub const hipMemPoolAttr_hipMemPoolAttrReservedMemHigh: hipMemPoolAttr = 6;
pub const hipMemPoolAttr_hipMemPoolAttrUsedMemCurrent: hipMemPoolAttr = 7;
pub const hipMemPoolAttr_hipMemPoolAttrUsedMemHigh: hipMemPoolAttr = 8;
pub type hipMemPoolAttr = ::std::os::raw::c_uint;
pub const hipMemAccessFlags_hipMemAccessFlagsProtNone: hipMemAccessFlags = 0;
pub const hipMemAccessFlags_hipMemAccessFlagsProtRead: hipMemAccessFlags = 1;
pub const hipMemAccessFlags_hipMemAccessFlagsProtReadWrite: hipMemAccessFlags = 3;
pub type hipMemAccessFlags = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemAccessDesc {
pub location: hipMemLocation,
pub flags: hipMemAccessFlags,
}
pub const hipMemAllocationType_hipMemAllocationTypeInvalid: hipMemAllocationType = 0;
pub const hipMemAllocationType_hipMemAllocationTypePinned: hipMemAllocationType = 1;
pub const hipMemAllocationType_hipMemAllocationTypeUncached: hipMemAllocationType = 1073741824;
pub const hipMemAllocationType_hipMemAllocationTypeMax: hipMemAllocationType = 2147483647;
pub type hipMemAllocationType = ::std::os::raw::c_uint;
pub const hipMemAllocationHandleType_hipMemHandleTypeNone: hipMemAllocationHandleType = 0;
pub const hipMemAllocationHandleType_hipMemHandleTypePosixFileDescriptor:
hipMemAllocationHandleType = 1;
pub const hipMemAllocationHandleType_hipMemHandleTypeWin32: hipMemAllocationHandleType = 2;
pub const hipMemAllocationHandleType_hipMemHandleTypeWin32Kmt: hipMemAllocationHandleType = 4;
pub type hipMemAllocationHandleType = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemPoolProps {
pub allocType: hipMemAllocationType,
pub handleTypes: hipMemAllocationHandleType,
pub location: hipMemLocation,
pub win32SecurityAttributes: *mut ::std::os::raw::c_void,
pub maxSize: usize,
pub reserved: [::std::os::raw::c_uchar; 56usize],
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemPoolPtrExportData {
pub reserved: [::std::os::raw::c_uchar; 64usize],
}
pub const hipFuncAttribute_hipFuncAttributeMaxDynamicSharedMemorySize: hipFuncAttribute = 8;
pub const hipFuncAttribute_hipFuncAttributePreferredSharedMemoryCarveout: hipFuncAttribute = 9;
pub const hipFuncAttribute_hipFuncAttributeMax: hipFuncAttribute = 10;
pub type hipFuncAttribute = ::std::os::raw::c_uint;
pub const hipFuncCache_t_hipFuncCachePreferNone: hipFuncCache_t = 0;
pub const hipFuncCache_t_hipFuncCachePreferShared: hipFuncCache_t = 1;
pub const hipFuncCache_t_hipFuncCachePreferL1: hipFuncCache_t = 2;
pub const hipFuncCache_t_hipFuncCachePreferEqual: hipFuncCache_t = 3;
pub type hipFuncCache_t = ::std::os::raw::c_uint;
pub const hipSharedMemConfig_hipSharedMemBankSizeDefault: hipSharedMemConfig = 0;
pub const hipSharedMemConfig_hipSharedMemBankSizeFourByte: hipSharedMemConfig = 1;
pub const hipSharedMemConfig_hipSharedMemBankSizeEightByte: hipSharedMemConfig = 2;
pub type hipSharedMemConfig = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct dim3 {
pub x: u32,
pub y: u32,
pub z: u32,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipLaunchParams_t {
pub func: *mut ::std::os::raw::c_void,
pub gridDim: dim3,
pub blockDim: dim3,
pub args: *mut *mut ::std::os::raw::c_void,
pub sharedMem: usize,
pub stream: hipStream_t,
}
pub type hipLaunchParams = hipLaunchParams_t;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipFunctionLaunchParams_t {
pub function: hipFunction_t,
pub gridDimX: ::std::os::raw::c_uint,
pub gridDimY: ::std::os::raw::c_uint,
pub gridDimZ: ::std::os::raw::c_uint,
pub blockDimX: ::std::os::raw::c_uint,
pub blockDimY: ::std::os::raw::c_uint,
pub blockDimZ: ::std::os::raw::c_uint,
pub sharedMemBytes: ::std::os::raw::c_uint,
pub hStream: hipStream_t,
pub kernelParams: *mut *mut ::std::os::raw::c_void,
}
pub type hipFunctionLaunchParams = hipFunctionLaunchParams_t;
pub const hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeOpaqueFd:
hipExternalMemoryHandleType_enum = 1;
pub const hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeOpaqueWin32:
hipExternalMemoryHandleType_enum = 2;
pub const hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeOpaqueWin32Kmt:
hipExternalMemoryHandleType_enum = 3;
pub const hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeD3D12Heap:
hipExternalMemoryHandleType_enum = 4;
pub const hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeD3D12Resource:
hipExternalMemoryHandleType_enum = 5;
pub const hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeD3D11Resource:
hipExternalMemoryHandleType_enum = 6;
pub const hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeD3D11ResourceKmt:
hipExternalMemoryHandleType_enum = 7;
pub const hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeNvSciBuf:
hipExternalMemoryHandleType_enum = 8;
pub type hipExternalMemoryHandleType_enum = ::std::os::raw::c_uint;
pub use self::hipExternalMemoryHandleType_enum as hipExternalMemoryHandleType;
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipExternalMemoryHandleDesc_st {
pub type_: hipExternalMemoryHandleType,
pub handle: hipExternalMemoryHandleDesc_st__bindgen_ty_1,
pub size: ::std::os::raw::c_ulonglong,
pub flags: ::std::os::raw::c_uint,
pub reserved: [::std::os::raw::c_uint; 16usize],
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipExternalMemoryHandleDesc_st__bindgen_ty_1 {
pub fd: ::std::os::raw::c_int,
pub win32: hipExternalMemoryHandleDesc_st__bindgen_ty_1__bindgen_ty_1,
pub nvSciBufObject: *const ::std::os::raw::c_void,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExternalMemoryHandleDesc_st__bindgen_ty_1__bindgen_ty_1 {
pub handle: *mut ::std::os::raw::c_void,
pub name: *const ::std::os::raw::c_void,
}
pub type hipExternalMemoryHandleDesc = hipExternalMemoryHandleDesc_st;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExternalMemoryBufferDesc_st {
pub offset: ::std::os::raw::c_ulonglong,
pub size: ::std::os::raw::c_ulonglong,
pub flags: ::std::os::raw::c_uint,
pub reserved: [::std::os::raw::c_uint; 16usize],
}
pub type hipExternalMemoryBufferDesc = hipExternalMemoryBufferDesc_st;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExternalMemoryMipmappedArrayDesc_st {
pub offset: ::std::os::raw::c_ulonglong,
pub formatDesc: hipChannelFormatDesc,
pub extent: hipExtent,
pub flags: ::std::os::raw::c_uint,
pub numLevels: ::std::os::raw::c_uint,
}
pub type hipExternalMemoryMipmappedArrayDesc = hipExternalMemoryMipmappedArrayDesc_st;
pub type hipExternalMemory_t = *mut ::std::os::raw::c_void;
pub const hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeOpaqueFd:
hipExternalSemaphoreHandleType_enum = 1;
pub const hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeOpaqueWin32:
hipExternalSemaphoreHandleType_enum = 2;
pub const hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeOpaqueWin32Kmt:
hipExternalSemaphoreHandleType_enum = 3;
pub const hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeD3D12Fence:
hipExternalSemaphoreHandleType_enum = 4;
pub const hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeD3D11Fence:
hipExternalSemaphoreHandleType_enum = 5;
pub const hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeNvSciSync:
hipExternalSemaphoreHandleType_enum = 6;
pub const hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeKeyedMutex:
hipExternalSemaphoreHandleType_enum = 7;
pub const hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeKeyedMutexKmt:
hipExternalSemaphoreHandleType_enum = 8;
pub const hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeTimelineSemaphoreFd:
hipExternalSemaphoreHandleType_enum = 9;
pub const hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeTimelineSemaphoreWin32 : hipExternalSemaphoreHandleType_enum = 10 ;
pub type hipExternalSemaphoreHandleType_enum = ::std::os::raw::c_uint;
pub use self::hipExternalSemaphoreHandleType_enum as hipExternalSemaphoreHandleType;
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipExternalSemaphoreHandleDesc_st {
pub type_: hipExternalSemaphoreHandleType,
pub handle: hipExternalSemaphoreHandleDesc_st__bindgen_ty_1,
pub flags: ::std::os::raw::c_uint,
pub reserved: [::std::os::raw::c_uint; 16usize],
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipExternalSemaphoreHandleDesc_st__bindgen_ty_1 {
pub fd: ::std::os::raw::c_int,
pub win32: hipExternalSemaphoreHandleDesc_st__bindgen_ty_1__bindgen_ty_1,
pub NvSciSyncObj: *const ::std::os::raw::c_void,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExternalSemaphoreHandleDesc_st__bindgen_ty_1__bindgen_ty_1 {
pub handle: *mut ::std::os::raw::c_void,
pub name: *const ::std::os::raw::c_void,
}
pub type hipExternalSemaphoreHandleDesc = hipExternalSemaphoreHandleDesc_st;
pub type hipExternalSemaphore_t = *mut ::std::os::raw::c_void;
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipExternalSemaphoreSignalParams_st {
pub params: hipExternalSemaphoreSignalParams_st__bindgen_ty_1,
pub flags: ::std::os::raw::c_uint,
pub reserved: [::std::os::raw::c_uint; 16usize],
}
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipExternalSemaphoreSignalParams_st__bindgen_ty_1 {
pub fence: hipExternalSemaphoreSignalParams_st__bindgen_ty_1__bindgen_ty_1,
pub nvSciSync: hipExternalSemaphoreSignalParams_st__bindgen_ty_1__bindgen_ty_2,
pub keyedMutex: hipExternalSemaphoreSignalParams_st__bindgen_ty_1__bindgen_ty_3,
pub reserved: [::std::os::raw::c_uint; 12usize],
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExternalSemaphoreSignalParams_st__bindgen_ty_1__bindgen_ty_1 {
pub value: ::std::os::raw::c_ulonglong,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipExternalSemaphoreSignalParams_st__bindgen_ty_1__bindgen_ty_2 {
pub fence: *mut ::std::os::raw::c_void,
pub reserved: ::std::os::raw::c_ulonglong,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExternalSemaphoreSignalParams_st__bindgen_ty_1__bindgen_ty_3 {
pub key: ::std::os::raw::c_ulonglong,
}
pub type hipExternalSemaphoreSignalParams = hipExternalSemaphoreSignalParams_st;
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipExternalSemaphoreWaitParams_st {
pub params: hipExternalSemaphoreWaitParams_st__bindgen_ty_1,
pub flags: ::std::os::raw::c_uint,
pub reserved: [::std::os::raw::c_uint; 16usize],
}
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipExternalSemaphoreWaitParams_st__bindgen_ty_1 {
pub fence: hipExternalSemaphoreWaitParams_st__bindgen_ty_1__bindgen_ty_1,
pub nvSciSync: hipExternalSemaphoreWaitParams_st__bindgen_ty_1__bindgen_ty_2,
pub keyedMutex: hipExternalSemaphoreWaitParams_st__bindgen_ty_1__bindgen_ty_3,
pub reserved: [::std::os::raw::c_uint; 10usize],
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExternalSemaphoreWaitParams_st__bindgen_ty_1__bindgen_ty_1 {
pub value: ::std::os::raw::c_ulonglong,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipExternalSemaphoreWaitParams_st__bindgen_ty_1__bindgen_ty_2 {
pub fence: *mut ::std::os::raw::c_void,
pub reserved: ::std::os::raw::c_ulonglong,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExternalSemaphoreWaitParams_st__bindgen_ty_1__bindgen_ty_3 {
pub key: ::std::os::raw::c_ulonglong,
pub timeoutMs: ::std::os::raw::c_uint,
}
pub type hipExternalSemaphoreWaitParams = hipExternalSemaphoreWaitParams_st;
pub const hipGraphicsRegisterFlags_hipGraphicsRegisterFlagsNone: hipGraphicsRegisterFlags = 0;
pub const hipGraphicsRegisterFlags_hipGraphicsRegisterFlagsReadOnly: hipGraphicsRegisterFlags = 1;
pub const hipGraphicsRegisterFlags_hipGraphicsRegisterFlagsWriteDiscard: hipGraphicsRegisterFlags =
2;
pub const hipGraphicsRegisterFlags_hipGraphicsRegisterFlagsSurfaceLoadStore:
hipGraphicsRegisterFlags = 4;
pub const hipGraphicsRegisterFlags_hipGraphicsRegisterFlagsTextureGather: hipGraphicsRegisterFlags =
8;
pub type hipGraphicsRegisterFlags = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct _hipGraphicsResource {
_unused: [u8; 0],
}
pub type hipGraphicsResource = _hipGraphicsResource;
pub type hipGraphicsResource_t = *mut hipGraphicsResource;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipGraph {
_unused: [u8; 0],
}
pub type hipGraph_t = *mut ihipGraph;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipGraphNode {
_unused: [u8; 0],
}
pub type hipGraphNode_t = *mut hipGraphNode;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipGraphExec {
_unused: [u8; 0],
}
pub type hipGraphExec_t = *mut hipGraphExec;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipUserObject {
_unused: [u8; 0],
}
pub type hipUserObject_t = *mut hipUserObject;
pub const hipGraphNodeType_hipGraphNodeTypeKernel: hipGraphNodeType = 0;
pub const hipGraphNodeType_hipGraphNodeTypeMemcpy: hipGraphNodeType = 1;
pub const hipGraphNodeType_hipGraphNodeTypeMemset: hipGraphNodeType = 2;
pub const hipGraphNodeType_hipGraphNodeTypeHost: hipGraphNodeType = 3;
pub const hipGraphNodeType_hipGraphNodeTypeGraph: hipGraphNodeType = 4;
pub const hipGraphNodeType_hipGraphNodeTypeEmpty: hipGraphNodeType = 5;
pub const hipGraphNodeType_hipGraphNodeTypeWaitEvent: hipGraphNodeType = 6;
pub const hipGraphNodeType_hipGraphNodeTypeEventRecord: hipGraphNodeType = 7;
pub const hipGraphNodeType_hipGraphNodeTypeExtSemaphoreSignal: hipGraphNodeType = 8;
pub const hipGraphNodeType_hipGraphNodeTypeExtSemaphoreWait: hipGraphNodeType = 9;
pub const hipGraphNodeType_hipGraphNodeTypeMemAlloc: hipGraphNodeType = 10;
pub const hipGraphNodeType_hipGraphNodeTypeMemFree: hipGraphNodeType = 11;
pub const hipGraphNodeType_hipGraphNodeTypeMemcpyFromSymbol: hipGraphNodeType = 12;
pub const hipGraphNodeType_hipGraphNodeTypeMemcpyToSymbol: hipGraphNodeType = 13;
pub const hipGraphNodeType_hipGraphNodeTypeBatchMemOp: hipGraphNodeType = 14;
pub const hipGraphNodeType_hipGraphNodeTypeCount: hipGraphNodeType = 15;
pub type hipGraphNodeType = ::std::os::raw::c_uint;
pub type hipHostFn_t =
::std::option::Option<unsafe extern "C" fn(userData: *mut ::std::os::raw::c_void)>;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipHostNodeParams {
pub fn_: hipHostFn_t,
pub userData: *mut ::std::os::raw::c_void,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipKernelNodeParams {
pub blockDim: dim3,
pub extra: *mut *mut ::std::os::raw::c_void,
pub func: *mut ::std::os::raw::c_void,
pub gridDim: dim3,
pub kernelParams: *mut *mut ::std::os::raw::c_void,
pub sharedMemBytes: ::std::os::raw::c_uint,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemsetParams {
pub dst: *mut ::std::os::raw::c_void,
pub elementSize: ::std::os::raw::c_uint,
pub height: usize,
pub pitch: usize,
pub value: ::std::os::raw::c_uint,
pub width: usize,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemAllocNodeParams {
pub poolProps: hipMemPoolProps,
pub accessDescs: *const hipMemAccessDesc,
pub accessDescCount: usize,
pub bytesize: usize,
pub dptr: *mut ::std::os::raw::c_void,
}
pub const hipAccessProperty_hipAccessPropertyNormal: hipAccessProperty = 0;
pub const hipAccessProperty_hipAccessPropertyStreaming: hipAccessProperty = 1;
pub const hipAccessProperty_hipAccessPropertyPersisting: hipAccessProperty = 2;
pub type hipAccessProperty = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipAccessPolicyWindow {
pub base_ptr: *mut ::std::os::raw::c_void,
pub hitProp: hipAccessProperty,
pub hitRatio: f32,
pub missProp: hipAccessProperty,
pub num_bytes: usize,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipLaunchMemSyncDomainMap {
pub default_: ::std::os::raw::c_uchar,
pub remote: ::std::os::raw::c_uchar,
}
pub const hipLaunchMemSyncDomain_hipLaunchMemSyncDomainDefault: hipLaunchMemSyncDomain = 0;
pub const hipLaunchMemSyncDomain_hipLaunchMemSyncDomainRemote: hipLaunchMemSyncDomain = 1;
pub type hipLaunchMemSyncDomain = ::std::os::raw::c_uint;
pub const hipSynchronizationPolicy_hipSyncPolicyAuto: hipSynchronizationPolicy = 1;
pub const hipSynchronizationPolicy_hipSyncPolicySpin: hipSynchronizationPolicy = 2;
pub const hipSynchronizationPolicy_hipSyncPolicyYield: hipSynchronizationPolicy = 3;
pub const hipSynchronizationPolicy_hipSyncPolicyBlockingSync: hipSynchronizationPolicy = 4;
pub type hipSynchronizationPolicy = ::std::os::raw::c_uint;
pub const hipLaunchAttributeID_hipLaunchAttributeAccessPolicyWindow: hipLaunchAttributeID = 1;
pub const hipLaunchAttributeID_hipLaunchAttributeCooperative: hipLaunchAttributeID = 2;
pub const hipLaunchAttributeID_hipLaunchAttributeSynchronizationPolicy: hipLaunchAttributeID = 3;
pub const hipLaunchAttributeID_hipLaunchAttributePriority: hipLaunchAttributeID = 8;
pub const hipLaunchAttributeID_hipLaunchAttributeMemSyncDomainMap: hipLaunchAttributeID = 9;
pub const hipLaunchAttributeID_hipLaunchAttributeMemSyncDomain: hipLaunchAttributeID = 10;
pub const hipLaunchAttributeID_hipLaunchAttributeMax: hipLaunchAttributeID = 11;
pub type hipLaunchAttributeID = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipLaunchAttributeValue {
pub pad: [::std::os::raw::c_char; 64usize],
pub accessPolicyWindow: hipAccessPolicyWindow,
pub cooperative: ::std::os::raw::c_int,
pub priority: ::std::os::raw::c_int,
pub syncPolicy: hipSynchronizationPolicy,
pub memSyncDomainMap: hipLaunchMemSyncDomainMap,
pub memSyncDomain: hipLaunchMemSyncDomain,
}
pub const hipGraphExecUpdateResult_hipGraphExecUpdateSuccess: hipGraphExecUpdateResult = 0;
pub const hipGraphExecUpdateResult_hipGraphExecUpdateError: hipGraphExecUpdateResult = 1;
pub const hipGraphExecUpdateResult_hipGraphExecUpdateErrorTopologyChanged:
hipGraphExecUpdateResult = 2;
pub const hipGraphExecUpdateResult_hipGraphExecUpdateErrorNodeTypeChanged:
hipGraphExecUpdateResult = 3;
pub const hipGraphExecUpdateResult_hipGraphExecUpdateErrorFunctionChanged:
hipGraphExecUpdateResult = 4;
pub const hipGraphExecUpdateResult_hipGraphExecUpdateErrorParametersChanged:
hipGraphExecUpdateResult = 5;
pub const hipGraphExecUpdateResult_hipGraphExecUpdateErrorNotSupported: hipGraphExecUpdateResult =
6;
pub const hipGraphExecUpdateResult_hipGraphExecUpdateErrorUnsupportedFunctionChange:
hipGraphExecUpdateResult = 7;
pub type hipGraphExecUpdateResult = ::std::os::raw::c_uint;
pub const hipStreamCaptureMode_hipStreamCaptureModeGlobal: hipStreamCaptureMode = 0;
pub const hipStreamCaptureMode_hipStreamCaptureModeThreadLocal: hipStreamCaptureMode = 1;
pub const hipStreamCaptureMode_hipStreamCaptureModeRelaxed: hipStreamCaptureMode = 2;
pub type hipStreamCaptureMode = ::std::os::raw::c_uint;
pub const hipStreamCaptureStatus_hipStreamCaptureStatusNone: hipStreamCaptureStatus = 0;
pub const hipStreamCaptureStatus_hipStreamCaptureStatusActive: hipStreamCaptureStatus = 1;
pub const hipStreamCaptureStatus_hipStreamCaptureStatusInvalidated: hipStreamCaptureStatus = 2;
pub type hipStreamCaptureStatus = ::std::os::raw::c_uint;
pub const hipStreamUpdateCaptureDependenciesFlags_hipStreamAddCaptureDependencies:
hipStreamUpdateCaptureDependenciesFlags = 0;
pub const hipStreamUpdateCaptureDependenciesFlags_hipStreamSetCaptureDependencies:
hipStreamUpdateCaptureDependenciesFlags = 1;
pub type hipStreamUpdateCaptureDependenciesFlags = ::std::os::raw::c_uint;
pub const hipGraphMemAttributeType_hipGraphMemAttrUsedMemCurrent: hipGraphMemAttributeType = 0;
pub const hipGraphMemAttributeType_hipGraphMemAttrUsedMemHigh: hipGraphMemAttributeType = 1;
pub const hipGraphMemAttributeType_hipGraphMemAttrReservedMemCurrent: hipGraphMemAttributeType = 2;
pub const hipGraphMemAttributeType_hipGraphMemAttrReservedMemHigh: hipGraphMemAttributeType = 3;
pub type hipGraphMemAttributeType = ::std::os::raw::c_uint;
pub const hipUserObjectFlags_hipUserObjectNoDestructorSync: hipUserObjectFlags = 1;
pub type hipUserObjectFlags = ::std::os::raw::c_uint;
pub const hipUserObjectRetainFlags_hipGraphUserObjectMove: hipUserObjectRetainFlags = 1;
pub type hipUserObjectRetainFlags = ::std::os::raw::c_uint;
pub const hipGraphInstantiateFlags_hipGraphInstantiateFlagAutoFreeOnLaunch:
hipGraphInstantiateFlags = 1;
pub const hipGraphInstantiateFlags_hipGraphInstantiateFlagUpload: hipGraphInstantiateFlags = 2;
pub const hipGraphInstantiateFlags_hipGraphInstantiateFlagDeviceLaunch: hipGraphInstantiateFlags =
4;
pub const hipGraphInstantiateFlags_hipGraphInstantiateFlagUseNodePriority:
hipGraphInstantiateFlags = 8;
pub type hipGraphInstantiateFlags = ::std::os::raw::c_uint;
pub const hipGraphDebugDotFlags_hipGraphDebugDotFlagsVerbose: hipGraphDebugDotFlags = 1;
pub const hipGraphDebugDotFlags_hipGraphDebugDotFlagsKernelNodeParams: hipGraphDebugDotFlags = 4;
pub const hipGraphDebugDotFlags_hipGraphDebugDotFlagsMemcpyNodeParams: hipGraphDebugDotFlags = 8;
pub const hipGraphDebugDotFlags_hipGraphDebugDotFlagsMemsetNodeParams: hipGraphDebugDotFlags = 16;
pub const hipGraphDebugDotFlags_hipGraphDebugDotFlagsHostNodeParams: hipGraphDebugDotFlags = 32;
pub const hipGraphDebugDotFlags_hipGraphDebugDotFlagsEventNodeParams: hipGraphDebugDotFlags = 64;
pub const hipGraphDebugDotFlags_hipGraphDebugDotFlagsExtSemasSignalNodeParams:
hipGraphDebugDotFlags = 128;
pub const hipGraphDebugDotFlags_hipGraphDebugDotFlagsExtSemasWaitNodeParams: hipGraphDebugDotFlags =
256;
pub const hipGraphDebugDotFlags_hipGraphDebugDotFlagsKernelNodeAttributes: hipGraphDebugDotFlags =
512;
pub const hipGraphDebugDotFlags_hipGraphDebugDotFlagsHandles: hipGraphDebugDotFlags = 1024;
pub type hipGraphDebugDotFlags = ::std::os::raw::c_uint;
pub const hipGraphInstantiateResult_hipGraphInstantiateSuccess: hipGraphInstantiateResult = 0;
pub const hipGraphInstantiateResult_hipGraphInstantiateError: hipGraphInstantiateResult = 1;
pub const hipGraphInstantiateResult_hipGraphInstantiateInvalidStructure: hipGraphInstantiateResult =
2;
pub const hipGraphInstantiateResult_hipGraphInstantiateNodeOperationNotSupported:
hipGraphInstantiateResult = 3;
pub const hipGraphInstantiateResult_hipGraphInstantiateMultipleDevicesNotSupported:
hipGraphInstantiateResult = 4;
pub type hipGraphInstantiateResult = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipGraphInstantiateParams {
pub errNode_out: hipGraphNode_t,
pub flags: ::std::os::raw::c_ulonglong,
pub result_out: hipGraphInstantiateResult,
pub uploadStream: hipStream_t,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipMemAllocationProp {
pub type_: hipMemAllocationType,
pub __bindgen_anon_1: hipMemAllocationProp__bindgen_ty_1,
pub location: hipMemLocation,
pub win32HandleMetaData: *mut ::std::os::raw::c_void,
pub allocFlags: hipMemAllocationProp__bindgen_ty_2,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipMemAllocationProp__bindgen_ty_1 {
pub requestedHandleType: hipMemAllocationHandleType,
pub requestedHandleTypes: hipMemAllocationHandleType,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemAllocationProp__bindgen_ty_2 {
pub compressionType: ::std::os::raw::c_uchar,
pub gpuDirectRDMACapable: ::std::os::raw::c_uchar,
pub usage: ::std::os::raw::c_ushort,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExternalSemaphoreSignalNodeParams {
pub extSemArray: *mut hipExternalSemaphore_t,
pub paramsArray: *const hipExternalSemaphoreSignalParams,
pub numExtSems: ::std::os::raw::c_uint,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipExternalSemaphoreWaitNodeParams {
pub extSemArray: *mut hipExternalSemaphore_t,
pub paramsArray: *const hipExternalSemaphoreWaitParams,
pub numExtSems: ::std::os::raw::c_uint,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct ihipMemGenericAllocationHandle {
_unused: [u8; 0],
}
pub type hipMemGenericAllocationHandle_t = *mut ihipMemGenericAllocationHandle;
pub const hipMemAllocationGranularity_flags_hipMemAllocationGranularityMinimum:
hipMemAllocationGranularity_flags = 0;
pub const hipMemAllocationGranularity_flags_hipMemAllocationGranularityRecommended:
hipMemAllocationGranularity_flags = 1;
pub type hipMemAllocationGranularity_flags = ::std::os::raw::c_uint;
pub const hipMemHandleType_hipMemHandleTypeGeneric: hipMemHandleType = 0;
pub type hipMemHandleType = ::std::os::raw::c_uint;
pub const hipMemOperationType_hipMemOperationTypeMap: hipMemOperationType = 1;
pub const hipMemOperationType_hipMemOperationTypeUnmap: hipMemOperationType = 2;
pub type hipMemOperationType = ::std::os::raw::c_uint;
pub const hipArraySparseSubresourceType_hipArraySparseSubresourceTypeSparseLevel:
hipArraySparseSubresourceType = 0;
pub const hipArraySparseSubresourceType_hipArraySparseSubresourceTypeMiptail:
hipArraySparseSubresourceType = 1;
pub type hipArraySparseSubresourceType = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipArrayMapInfo {
pub resourceType: hipResourceType,
pub resource: hipArrayMapInfo__bindgen_ty_1,
pub subresourceType: hipArraySparseSubresourceType,
pub subresource: hipArrayMapInfo__bindgen_ty_2,
pub memOperationType: hipMemOperationType,
pub memHandleType: hipMemHandleType,
pub memHandle: hipArrayMapInfo__bindgen_ty_3,
pub offset: ::std::os::raw::c_ulonglong,
pub deviceBitMask: ::std::os::raw::c_uint,
pub flags: ::std::os::raw::c_uint,
pub reserved: [::std::os::raw::c_uint; 2usize],
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipArrayMapInfo__bindgen_ty_1 {
pub mipmap: hipMipmappedArray,
pub array: hipArray_t,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipArrayMapInfo__bindgen_ty_2 {
pub sparseLevel: hipArrayMapInfo__bindgen_ty_2__bindgen_ty_1,
pub miptail: hipArrayMapInfo__bindgen_ty_2__bindgen_ty_2,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipArrayMapInfo__bindgen_ty_2__bindgen_ty_1 {
pub level: ::std::os::raw::c_uint,
pub layer: ::std::os::raw::c_uint,
pub offsetX: ::std::os::raw::c_uint,
pub offsetY: ::std::os::raw::c_uint,
pub offsetZ: ::std::os::raw::c_uint,
pub extentWidth: ::std::os::raw::c_uint,
pub extentHeight: ::std::os::raw::c_uint,
pub extentDepth: ::std::os::raw::c_uint,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipArrayMapInfo__bindgen_ty_2__bindgen_ty_2 {
pub layer: ::std::os::raw::c_uint,
pub offset: ::std::os::raw::c_ulonglong,
pub size: ::std::os::raw::c_ulonglong,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipArrayMapInfo__bindgen_ty_3 {
pub memHandle: hipMemGenericAllocationHandle_t,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemcpyNodeParams {
pub flags: ::std::os::raw::c_int,
pub reserved: [::std::os::raw::c_int; 3usize],
pub copyParams: hipMemcpy3DParms,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipChildGraphNodeParams {
pub graph: hipGraph_t,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipEventWaitNodeParams {
pub event: hipEvent_t,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipEventRecordNodeParams {
pub event: hipEvent_t,
}
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipMemFreeNodeParams {
pub dptr: *mut ::std::os::raw::c_void,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipGraphNodeParams {
pub type_: hipGraphNodeType,
pub reserved0: [::std::os::raw::c_int; 3usize],
pub __bindgen_anon_1: hipGraphNodeParams__bindgen_ty_1,
pub reserved2: ::std::os::raw::c_longlong,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipGraphNodeParams__bindgen_ty_1 {
pub reserved1: [::std::os::raw::c_longlong; 29usize],
pub kernel: hipKernelNodeParams,
pub memcpy: hipMemcpyNodeParams,
pub memset: hipMemsetParams,
pub host: hipHostNodeParams,
pub graph: hipChildGraphNodeParams,
pub eventWait: hipEventWaitNodeParams,
pub eventRecord: hipEventRecordNodeParams,
pub extSemSignal: hipExternalSemaphoreSignalNodeParams,
pub extSemWait: hipExternalSemaphoreWaitNodeParams,
pub alloc: hipMemAllocNodeParams,
pub free: hipMemFreeNodeParams,
}
pub const hipGraphDependencyType_hipGraphDependencyTypeDefault: hipGraphDependencyType = 0;
pub const hipGraphDependencyType_hipGraphDependencyTypeProgrammatic: hipGraphDependencyType = 1;
pub type hipGraphDependencyType = ::std::os::raw::c_uint;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipGraphEdgeData {
pub from_port: ::std::os::raw::c_uchar,
pub reserved: [::std::os::raw::c_uchar; 5usize],
pub to_port: ::std::os::raw::c_uchar,
pub type_: ::std::os::raw::c_uchar,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub struct hipLaunchAttribute_st {
pub id: hipLaunchAttributeID,
pub pad: [::std::os::raw::c_char; 4usize],
pub __bindgen_anon_1: hipLaunchAttribute_st__bindgen_ty_1,
}
#[repr(C)]
#[derive(Copy, Clone)]
pub union hipLaunchAttribute_st__bindgen_ty_1 {
pub val: hipLaunchAttributeValue,
pub value: hipLaunchAttributeValue,
}
pub type hipLaunchAttribute = hipLaunchAttribute_st;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct hipLaunchConfig_st {
pub gridDim: dim3,
pub blockDim: dim3,
pub dynamicSmemBytes: usize,
pub stream: hipStream_t,
pub attrs: *mut hipLaunchAttribute,
pub numAttrs: ::std::os::raw::c_uint,
}
pub type hipLaunchConfig_t = hipLaunchConfig_st;
#[repr(C)]
#[derive(Debug, Copy, Clone)]
pub struct HIP_LAUNCH_CONFIG_st {
pub gridDimX: ::std::os::raw::c_uint,
pub gridDimY: ::std::os::raw::c_uint,
pub gridDimZ: ::std::os::raw::c_uint,
pub blockDimX: ::std::os::raw::c_uint,
pub blockDimY: ::std::os::raw::c_uint,
pub blockDimZ: ::std::os::raw::c_uint,
pub sharedMemBytes: ::std::os::raw::c_uint,
pub hStream: hipStream_t,
pub attrs: *mut hipLaunchAttribute,
pub numAttrs: ::std::os::raw::c_uint,
}
pub type HIP_LAUNCH_CONFIG = HIP_LAUNCH_CONFIG_st;
pub const hipMemRangeHandleType_hipMemRangeHandleTypeDmaBufFd: hipMemRangeHandleType = 1;
pub const hipMemRangeHandleType_hipMemRangeHandleTypeMax: hipMemRangeHandleType = 2147483647;
pub type hipMemRangeHandleType = ::std::os::raw::c_uint;
pub const hipMemRangeFlags_hipMemRangeFlagDmaBufMappingTypePcie: hipMemRangeFlags = 1;
pub const hipMemRangeFlags_hipMemRangeFlagsMax: hipMemRangeFlags = 2147483647;
pub type hipMemRangeFlags = ::std::os::raw::c_uint;
unsafe extern "C" {
pub fn hipInit(flags: ::std::os::raw::c_uint) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDriverGetVersion(driverVersion: *mut ::std::os::raw::c_int) -> hipError_t;
}
unsafe extern "C" {
pub fn hipRuntimeGetVersion(runtimeVersion: *mut ::std::os::raw::c_int) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGet(device: *mut hipDevice_t, ordinal: ::std::os::raw::c_int) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceComputeCapability(
major: *mut ::std::os::raw::c_int,
minor: *mut ::std::os::raw::c_int,
device: hipDevice_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetName(
name: *mut ::std::os::raw::c_char,
len: ::std::os::raw::c_int,
device: hipDevice_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetUuid(uuid: *mut hipUUID, device: hipDevice_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetP2PAttribute(
value: *mut ::std::os::raw::c_int,
attr: hipDeviceP2PAttr,
srcDevice: ::std::os::raw::c_int,
dstDevice: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetPCIBusId(
pciBusId: *mut ::std::os::raw::c_char,
len: ::std::os::raw::c_int,
device: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetByPCIBusId(
device: *mut ::std::os::raw::c_int,
pciBusId: *const ::std::os::raw::c_char,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceTotalMem(bytes: *mut usize, device: hipDevice_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceSynchronize() -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceReset() -> hipError_t;
}
unsafe extern "C" {
pub fn hipSetDevice(deviceId: ::std::os::raw::c_int) -> hipError_t;
}
unsafe extern "C" {
pub fn hipSetValidDevices(
device_arr: *mut ::std::os::raw::c_int,
len: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetDevice(deviceId: *mut ::std::os::raw::c_int) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetDeviceCount(count: *mut ::std::os::raw::c_int) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetAttribute(
pi: *mut ::std::os::raw::c_int,
attr: hipDeviceAttribute_t,
deviceId: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetDefaultMemPool(
mem_pool: *mut hipMemPool_t,
device: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceSetMemPool(device: ::std::os::raw::c_int, mem_pool: hipMemPool_t)
-> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetMemPool(
mem_pool: *mut hipMemPool_t,
device: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetDevicePropertiesR0600(
prop: *mut hipDeviceProp_tR0600,
deviceId: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetTexture1DLinearMaxWidth(
max_width: *mut usize,
desc: *const hipChannelFormatDesc,
device: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceSetCacheConfig(cacheConfig: hipFuncCache_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetCacheConfig(cacheConfig: *mut hipFuncCache_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetLimit(pValue: *mut usize, limit: hipLimit_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceSetLimit(limit: hipLimit_t, value: usize) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetSharedMemConfig(pConfig: *mut hipSharedMemConfig) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetDeviceFlags(flags: *mut ::std::os::raw::c_uint) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceSetSharedMemConfig(config: hipSharedMemConfig) -> hipError_t;
}
unsafe extern "C" {
pub fn hipSetDeviceFlags(flags: ::std::os::raw::c_uint) -> hipError_t;
}
unsafe extern "C" {
pub fn hipChooseDeviceR0600(
device: *mut ::std::os::raw::c_int,
prop: *const hipDeviceProp_tR0600,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipExtGetLinkTypeAndHopCount(
device1: ::std::os::raw::c_int,
device2: ::std::os::raw::c_int,
linktype: *mut u32,
hopcount: *mut u32,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipIpcGetMemHandle(
handle: *mut hipIpcMemHandle_t,
devPtr: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipIpcOpenMemHandle(
devPtr: *mut *mut ::std::os::raw::c_void,
handle: hipIpcMemHandle_t,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipIpcCloseMemHandle(devPtr: *mut ::std::os::raw::c_void) -> hipError_t;
}
unsafe extern "C" {
pub fn hipIpcGetEventHandle(handle: *mut hipIpcEventHandle_t, event: hipEvent_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipIpcOpenEventHandle(event: *mut hipEvent_t, handle: hipIpcEventHandle_t)
-> hipError_t;
}
unsafe extern "C" {
pub fn hipFuncSetAttribute(
func: *const ::std::os::raw::c_void,
attr: hipFuncAttribute,
value: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipFuncSetCacheConfig(
func: *const ::std::os::raw::c_void,
config: hipFuncCache_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipFuncSetSharedMemConfig(
func: *const ::std::os::raw::c_void,
config: hipSharedMemConfig,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetLastError() -> hipError_t;
}
unsafe extern "C" {
pub fn hipExtGetLastError() -> hipError_t;
}
unsafe extern "C" {
pub fn hipPeekAtLastError() -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetErrorName(hip_error: hipError_t) -> *const ::std::os::raw::c_char;
}
unsafe extern "C" {
pub fn hipGetErrorString(hipError: hipError_t) -> *const ::std::os::raw::c_char;
}
unsafe extern "C" {
pub fn hipDrvGetErrorName(
hipError: hipError_t,
errorString: *mut *const ::std::os::raw::c_char,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvGetErrorString(
hipError: hipError_t,
errorString: *mut *const ::std::os::raw::c_char,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamCreate(stream: *mut hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamCreateWithFlags(
stream: *mut hipStream_t,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamCreateWithPriority(
stream: *mut hipStream_t,
flags: ::std::os::raw::c_uint,
priority: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetStreamPriorityRange(
leastPriority: *mut ::std::os::raw::c_int,
greatestPriority: *mut ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamDestroy(stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamQuery(stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamSynchronize(stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamWaitEvent(
stream: hipStream_t,
event: hipEvent_t,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetFlags(stream: hipStream_t, flags: *mut ::std::os::raw::c_uint)
-> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetId(
stream: hipStream_t,
streamId: *mut ::std::os::raw::c_ulonglong,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetPriority(
stream: hipStream_t,
priority: *mut ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetDevice(stream: hipStream_t, device: *mut hipDevice_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipExtStreamCreateWithCUMask(
stream: *mut hipStream_t,
cuMaskSize: u32,
cuMask: *const u32,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipExtStreamGetCUMask(
stream: hipStream_t,
cuMaskSize: u32,
cuMask: *mut u32,
) -> hipError_t;
}
pub type hipStreamCallback_t = ::std::option::Option<
unsafe extern "C" fn(
stream: hipStream_t,
status: hipError_t,
userData: *mut ::std::os::raw::c_void,
),
>;
unsafe extern "C" {
pub fn hipStreamAddCallback(
stream: hipStream_t,
callback: hipStreamCallback_t,
userData: *mut ::std::os::raw::c_void,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamSetAttribute(
stream: hipStream_t,
attr: hipLaunchAttributeID,
value: *const hipLaunchAttributeValue,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetAttribute(
stream: hipStream_t,
attr: hipLaunchAttributeID,
value_out: *mut hipLaunchAttributeValue,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamWaitValue32(
stream: hipStream_t,
ptr: *mut ::std::os::raw::c_void,
value: u32,
flags: ::std::os::raw::c_uint,
mask: u32,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamWaitValue64(
stream: hipStream_t,
ptr: *mut ::std::os::raw::c_void,
value: u64,
flags: ::std::os::raw::c_uint,
mask: u64,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamWriteValue32(
stream: hipStream_t,
ptr: *mut ::std::os::raw::c_void,
value: u32,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamWriteValue64(
stream: hipStream_t,
ptr: *mut ::std::os::raw::c_void,
value: u64,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamBatchMemOp(
stream: hipStream_t,
count: ::std::os::raw::c_uint,
paramArray: *mut hipStreamBatchMemOpParams,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddBatchMemOpNode(
phGraphNode: *mut hipGraphNode_t,
hGraph: hipGraph_t,
dependencies: *const hipGraphNode_t,
numDependencies: usize,
nodeParams: *const hipBatchMemOpNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphBatchMemOpNodeGetParams(
hNode: hipGraphNode_t,
nodeParams_out: *mut hipBatchMemOpNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphBatchMemOpNodeSetParams(
hNode: hipGraphNode_t,
nodeParams: *mut hipBatchMemOpNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecBatchMemOpNodeSetParams(
hGraphExec: hipGraphExec_t,
hNode: hipGraphNode_t,
nodeParams: *const hipBatchMemOpNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipEventCreateWithFlags(
event: *mut hipEvent_t,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipEventCreate(event: *mut hipEvent_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipEventRecordWithFlags(
event: hipEvent_t,
stream: hipStream_t,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipEventRecord(event: hipEvent_t, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipEventDestroy(event: hipEvent_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipEventSynchronize(event: hipEvent_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipEventElapsedTime(ms: *mut f32, start: hipEvent_t, stop: hipEvent_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipEventQuery(event: hipEvent_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipPointerSetAttribute(
value: *const ::std::os::raw::c_void,
attribute: hipPointer_attribute,
ptr: hipDeviceptr_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipPointerGetAttributes(
attributes: *mut hipPointerAttribute_t,
ptr: *const ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipPointerGetAttribute(
data: *mut ::std::os::raw::c_void,
attribute: hipPointer_attribute,
ptr: hipDeviceptr_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvPointerGetAttributes(
numAttributes: ::std::os::raw::c_uint,
attributes: *mut hipPointer_attribute,
data: *mut *mut ::std::os::raw::c_void,
ptr: hipDeviceptr_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipImportExternalSemaphore(
extSem_out: *mut hipExternalSemaphore_t,
semHandleDesc: *const hipExternalSemaphoreHandleDesc,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipSignalExternalSemaphoresAsync(
extSemArray: *const hipExternalSemaphore_t,
paramsArray: *const hipExternalSemaphoreSignalParams,
numExtSems: ::std::os::raw::c_uint,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipWaitExternalSemaphoresAsync(
extSemArray: *const hipExternalSemaphore_t,
paramsArray: *const hipExternalSemaphoreWaitParams,
numExtSems: ::std::os::raw::c_uint,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDestroyExternalSemaphore(extSem: hipExternalSemaphore_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipImportExternalMemory(
extMem_out: *mut hipExternalMemory_t,
memHandleDesc: *const hipExternalMemoryHandleDesc,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipExternalMemoryGetMappedBuffer(
devPtr: *mut *mut ::std::os::raw::c_void,
extMem: hipExternalMemory_t,
bufferDesc: *const hipExternalMemoryBufferDesc,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDestroyExternalMemory(extMem: hipExternalMemory_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipExternalMemoryGetMappedMipmappedArray(
mipmap: *mut hipMipmappedArray_t,
extMem: hipExternalMemory_t,
mipmapDesc: *const hipExternalMemoryMipmappedArrayDesc,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMalloc(ptr: *mut *mut ::std::os::raw::c_void, size: usize) -> hipError_t;
}
unsafe extern "C" {
pub fn hipExtMallocWithFlags(
ptr: *mut *mut ::std::os::raw::c_void,
sizeBytes: usize,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMallocHost(ptr: *mut *mut ::std::os::raw::c_void, size: usize) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemAllocHost(ptr: *mut *mut ::std::os::raw::c_void, size: usize) -> hipError_t;
}
unsafe extern "C" {
pub fn hipHostMalloc(
ptr: *mut *mut ::std::os::raw::c_void,
size: usize,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMallocManaged(
dev_ptr: *mut *mut ::std::os::raw::c_void,
size: usize,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPrefetchAsync(
dev_ptr: *const ::std::os::raw::c_void,
count: usize,
device: ::std::os::raw::c_int,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPrefetchAsync_v2(
dev_ptr: *const ::std::os::raw::c_void,
count: usize,
location: hipMemLocation,
flags: ::std::os::raw::c_uint,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemAdvise(
dev_ptr: *const ::std::os::raw::c_void,
count: usize,
advice: hipMemoryAdvise,
device: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemAdvise_v2(
dev_ptr: *const ::std::os::raw::c_void,
count: usize,
advice: hipMemoryAdvise,
location: hipMemLocation,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemRangeGetAttribute(
data: *mut ::std::os::raw::c_void,
data_size: usize,
attribute: hipMemRangeAttribute,
dev_ptr: *const ::std::os::raw::c_void,
count: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemRangeGetAttributes(
data: *mut *mut ::std::os::raw::c_void,
data_sizes: *mut usize,
attributes: *mut hipMemRangeAttribute,
num_attributes: usize,
dev_ptr: *const ::std::os::raw::c_void,
count: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamAttachMemAsync(
stream: hipStream_t,
dev_ptr: *mut ::std::os::raw::c_void,
length: usize,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMallocAsync(
dev_ptr: *mut *mut ::std::os::raw::c_void,
size: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipFreeAsync(dev_ptr: *mut ::std::os::raw::c_void, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolTrimTo(mem_pool: hipMemPool_t, min_bytes_to_hold: usize) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolSetAttribute(
mem_pool: hipMemPool_t,
attr: hipMemPoolAttr,
value: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolGetAttribute(
mem_pool: hipMemPool_t,
attr: hipMemPoolAttr,
value: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolSetAccess(
mem_pool: hipMemPool_t,
desc_list: *const hipMemAccessDesc,
count: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolGetAccess(
flags: *mut hipMemAccessFlags,
mem_pool: hipMemPool_t,
location: *mut hipMemLocation,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolCreate(
mem_pool: *mut hipMemPool_t,
pool_props: *const hipMemPoolProps,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolDestroy(mem_pool: hipMemPool_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMallocFromPoolAsync(
dev_ptr: *mut *mut ::std::os::raw::c_void,
size: usize,
mem_pool: hipMemPool_t,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolExportToShareableHandle(
shared_handle: *mut ::std::os::raw::c_void,
mem_pool: hipMemPool_t,
handle_type: hipMemAllocationHandleType,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolImportFromShareableHandle(
mem_pool: *mut hipMemPool_t,
shared_handle: *mut ::std::os::raw::c_void,
handle_type: hipMemAllocationHandleType,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolExportPointer(
export_data: *mut hipMemPoolPtrExportData,
dev_ptr: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPoolImportPointer(
dev_ptr: *mut *mut ::std::os::raw::c_void,
mem_pool: hipMemPool_t,
export_data: *mut hipMemPoolPtrExportData,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipHostAlloc(
ptr: *mut *mut ::std::os::raw::c_void,
size: usize,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipHostGetDevicePointer(
devPtr: *mut *mut ::std::os::raw::c_void,
hstPtr: *mut ::std::os::raw::c_void,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipHostGetFlags(
flagsPtr: *mut ::std::os::raw::c_uint,
hostPtr: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipHostRegister(
hostPtr: *mut ::std::os::raw::c_void,
sizeBytes: usize,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipHostUnregister(hostPtr: *mut ::std::os::raw::c_void) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMallocPitch(
ptr: *mut *mut ::std::os::raw::c_void,
pitch: *mut usize,
width: usize,
height: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemAllocPitch(
dptr: *mut hipDeviceptr_t,
pitch: *mut usize,
widthInBytes: usize,
height: usize,
elementSizeBytes: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipFree(ptr: *mut ::std::os::raw::c_void) -> hipError_t;
}
unsafe extern "C" {
pub fn hipFreeHost(ptr: *mut ::std::os::raw::c_void) -> hipError_t;
}
unsafe extern "C" {
pub fn hipHostFree(ptr: *mut ::std::os::raw::c_void) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy(
dst: *mut ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyWithStream(
dst: *mut ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyHtoD(
dst: hipDeviceptr_t,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyDtoH(
dst: *mut ::std::os::raw::c_void,
src: hipDeviceptr_t,
sizeBytes: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyDtoD(dst: hipDeviceptr_t, src: hipDeviceptr_t, sizeBytes: usize) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyAtoD(
dstDevice: hipDeviceptr_t,
srcArray: hipArray_t,
srcOffset: usize,
ByteCount: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyDtoA(
dstArray: hipArray_t,
dstOffset: usize,
srcDevice: hipDeviceptr_t,
ByteCount: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyAtoA(
dstArray: hipArray_t,
dstOffset: usize,
srcArray: hipArray_t,
srcOffset: usize,
ByteCount: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyHtoDAsync(
dst: hipDeviceptr_t,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyDtoHAsync(
dst: *mut ::std::os::raw::c_void,
src: hipDeviceptr_t,
sizeBytes: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyDtoDAsync(
dst: hipDeviceptr_t,
src: hipDeviceptr_t,
sizeBytes: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyAtoHAsync(
dstHost: *mut ::std::os::raw::c_void,
srcArray: hipArray_t,
srcOffset: usize,
ByteCount: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyHtoAAsync(
dstArray: hipArray_t,
dstOffset: usize,
srcHost: *const ::std::os::raw::c_void,
ByteCount: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleGetGlobal(
dptr: *mut hipDeviceptr_t,
bytes: *mut usize,
hmod: hipModule_t,
name: *const ::std::os::raw::c_char,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetSymbolAddress(
devPtr: *mut *mut ::std::os::raw::c_void,
symbol: *const ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetSymbolSize(size: *mut usize, symbol: *const ::std::os::raw::c_void) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetProcAddress(
symbol: *const ::std::os::raw::c_char,
pfn: *mut *mut ::std::os::raw::c_void,
hipVersion: ::std::os::raw::c_int,
flags: u64,
symbolStatus: *mut hipDriverProcAddressQueryResult,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyToSymbol(
symbol: *const ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
offset: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyToSymbolAsync(
symbol: *const ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
offset: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyFromSymbol(
dst: *mut ::std::os::raw::c_void,
symbol: *const ::std::os::raw::c_void,
sizeBytes: usize,
offset: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyFromSymbolAsync(
dst: *mut ::std::os::raw::c_void,
symbol: *const ::std::os::raw::c_void,
sizeBytes: usize,
offset: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyAsync(
dst: *mut ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemset(
dst: *mut ::std::os::raw::c_void,
value: ::std::os::raw::c_int,
sizeBytes: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD8(
dest: hipDeviceptr_t,
value: ::std::os::raw::c_uchar,
count: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD8Async(
dest: hipDeviceptr_t,
value: ::std::os::raw::c_uchar,
count: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD16(
dest: hipDeviceptr_t,
value: ::std::os::raw::c_ushort,
count: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD16Async(
dest: hipDeviceptr_t,
value: ::std::os::raw::c_ushort,
count: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD32(
dest: hipDeviceptr_t,
value: ::std::os::raw::c_int,
count: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetAsync(
dst: *mut ::std::os::raw::c_void,
value: ::std::os::raw::c_int,
sizeBytes: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD32Async(
dst: hipDeviceptr_t,
value: ::std::os::raw::c_int,
count: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemset2D(
dst: *mut ::std::os::raw::c_void,
pitch: usize,
value: ::std::os::raw::c_int,
width: usize,
height: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemset2DAsync(
dst: *mut ::std::os::raw::c_void,
pitch: usize,
value: ::std::os::raw::c_int,
width: usize,
height: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemset3D(
pitchedDevPtr: hipPitchedPtr,
value: ::std::os::raw::c_int,
extent: hipExtent,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemset3DAsync(
pitchedDevPtr: hipPitchedPtr,
value: ::std::os::raw::c_int,
extent: hipExtent,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD2D8(
dst: hipDeviceptr_t,
dstPitch: usize,
value: ::std::os::raw::c_uchar,
width: usize,
height: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD2D8Async(
dst: hipDeviceptr_t,
dstPitch: usize,
value: ::std::os::raw::c_uchar,
width: usize,
height: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD2D16(
dst: hipDeviceptr_t,
dstPitch: usize,
value: ::std::os::raw::c_ushort,
width: usize,
height: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD2D16Async(
dst: hipDeviceptr_t,
dstPitch: usize,
value: ::std::os::raw::c_ushort,
width: usize,
height: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD2D32(
dst: hipDeviceptr_t,
dstPitch: usize,
value: ::std::os::raw::c_uint,
width: usize,
height: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetD2D32Async(
dst: hipDeviceptr_t,
dstPitch: usize,
value: ::std::os::raw::c_uint,
width: usize,
height: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemGetInfo(free: *mut usize, total: *mut usize) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemPtrGetInfo(ptr: *mut ::std::os::raw::c_void, size: *mut usize) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMallocArray(
array: *mut hipArray_t,
desc: *const hipChannelFormatDesc,
width: usize,
height: usize,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipArrayCreate(
pHandle: *mut hipArray_t,
pAllocateArray: *const HIP_ARRAY_DESCRIPTOR,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipArrayDestroy(array: hipArray_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipArray3DCreate(
array: *mut hipArray_t,
pAllocateArray: *const HIP_ARRAY3D_DESCRIPTOR,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMalloc3D(pitchedDevPtr: *mut hipPitchedPtr, extent: hipExtent) -> hipError_t;
}
unsafe extern "C" {
pub fn hipFreeArray(array: hipArray_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMalloc3DArray(
array: *mut hipArray_t,
desc: *const hipChannelFormatDesc,
extent: hipExtent,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipArrayGetInfo(
desc: *mut hipChannelFormatDesc,
extent: *mut hipExtent,
flags: *mut ::std::os::raw::c_uint,
array: hipArray_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipArrayGetDescriptor(
pArrayDescriptor: *mut HIP_ARRAY_DESCRIPTOR,
array: hipArray_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipArray3DGetDescriptor(
pArrayDescriptor: *mut HIP_ARRAY3D_DESCRIPTOR,
array: hipArray_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2D(
dst: *mut ::std::os::raw::c_void,
dpitch: usize,
src: *const ::std::os::raw::c_void,
spitch: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyParam2D(pCopy: *const hip_Memcpy2D) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyParam2DAsync(pCopy: *const hip_Memcpy2D, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DAsync(
dst: *mut ::std::os::raw::c_void,
dpitch: usize,
src: *const ::std::os::raw::c_void,
spitch: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DToArray(
dst: hipArray_t,
wOffset: usize,
hOffset: usize,
src: *const ::std::os::raw::c_void,
spitch: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DToArrayAsync(
dst: hipArray_t,
wOffset: usize,
hOffset: usize,
src: *const ::std::os::raw::c_void,
spitch: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DArrayToArray(
dst: hipArray_t,
wOffsetDst: usize,
hOffsetDst: usize,
src: hipArray_const_t,
wOffsetSrc: usize,
hOffsetSrc: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyToArray(
dst: hipArray_t,
wOffset: usize,
hOffset: usize,
src: *const ::std::os::raw::c_void,
count: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyFromArray(
dst: *mut ::std::os::raw::c_void,
srcArray: hipArray_const_t,
wOffset: usize,
hOffset: usize,
count: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DFromArray(
dst: *mut ::std::os::raw::c_void,
dpitch: usize,
src: hipArray_const_t,
wOffset: usize,
hOffset: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DFromArrayAsync(
dst: *mut ::std::os::raw::c_void,
dpitch: usize,
src: hipArray_const_t,
wOffset: usize,
hOffset: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyAtoH(
dst: *mut ::std::os::raw::c_void,
srcArray: hipArray_t,
srcOffset: usize,
count: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyHtoA(
dstArray: hipArray_t,
dstOffset: usize,
srcHost: *const ::std::os::raw::c_void,
count: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy3D(p: *const hipMemcpy3DParms) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy3DAsync(p: *const hipMemcpy3DParms, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvMemcpy3D(pCopy: *const HIP_MEMCPY3D) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvMemcpy3DAsync(pCopy: *const HIP_MEMCPY3D, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemGetAddressRange(
pbase: *mut hipDeviceptr_t,
psize: *mut usize,
dptr: hipDeviceptr_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyBatchAsync(
dsts: *mut *mut ::std::os::raw::c_void,
srcs: *mut *mut ::std::os::raw::c_void,
sizes: *mut usize,
count: usize,
attrs: *mut hipMemcpyAttributes,
attrsIdxs: *mut usize,
numAttrs: usize,
failIdx: *mut usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy3DBatchAsync(
numOps: usize,
opList: *mut hipMemcpy3DBatchOp,
failIdx: *mut usize,
flags: ::std::os::raw::c_ulonglong,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy3DPeer(p: *mut hipMemcpy3DPeerParms) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy3DPeerAsync(p: *mut hipMemcpy3DPeerParms, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceCanAccessPeer(
canAccessPeer: *mut ::std::os::raw::c_int,
deviceId: ::std::os::raw::c_int,
peerDeviceId: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceEnablePeerAccess(
peerDeviceId: ::std::os::raw::c_int,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceDisablePeerAccess(peerDeviceId: ::std::os::raw::c_int) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyPeer(
dst: *mut ::std::os::raw::c_void,
dstDeviceId: ::std::os::raw::c_int,
src: *const ::std::os::raw::c_void,
srcDeviceId: ::std::os::raw::c_int,
sizeBytes: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyPeerAsync(
dst: *mut ::std::os::raw::c_void,
dstDeviceId: ::std::os::raw::c_int,
src: *const ::std::os::raw::c_void,
srcDevice: ::std::os::raw::c_int,
sizeBytes: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxCreate(
ctx: *mut hipCtx_t,
flags: ::std::os::raw::c_uint,
device: hipDevice_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxDestroy(ctx: hipCtx_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxPopCurrent(ctx: *mut hipCtx_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxPushCurrent(ctx: hipCtx_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxSetCurrent(ctx: hipCtx_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxGetCurrent(ctx: *mut hipCtx_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxGetDevice(device: *mut hipDevice_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxGetApiVersion(
ctx: hipCtx_t,
apiVersion: *mut ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxGetCacheConfig(cacheConfig: *mut hipFuncCache_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxSetCacheConfig(cacheConfig: hipFuncCache_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxSetSharedMemConfig(config: hipSharedMemConfig) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxGetSharedMemConfig(pConfig: *mut hipSharedMemConfig) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxSynchronize() -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxGetFlags(flags: *mut ::std::os::raw::c_uint) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxEnablePeerAccess(peerCtx: hipCtx_t, flags: ::std::os::raw::c_uint) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCtxDisablePeerAccess(peerCtx: hipCtx_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDevicePrimaryCtxGetState(
dev: hipDevice_t,
flags: *mut ::std::os::raw::c_uint,
active: *mut ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDevicePrimaryCtxRelease(dev: hipDevice_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDevicePrimaryCtxRetain(pctx: *mut hipCtx_t, dev: hipDevice_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDevicePrimaryCtxReset(dev: hipDevice_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDevicePrimaryCtxSetFlags(
dev: hipDevice_t,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleLoadFatBinary(
module: *mut hipModule_t,
fatbin: *const ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleLoad(
module: *mut hipModule_t,
fname: *const ::std::os::raw::c_char,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleUnload(module: hipModule_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleGetFunction(
function: *mut hipFunction_t,
module: hipModule_t,
kname: *const ::std::os::raw::c_char,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleGetFunctionCount(
count: *mut ::std::os::raw::c_uint,
mod_: hipModule_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLibraryLoadData(
library: *mut hipLibrary_t,
code: *const ::std::os::raw::c_void,
jitOptions: *mut hipJitOption,
jitOptionsValues: *mut *mut ::std::os::raw::c_void,
numJitOptions: ::std::os::raw::c_uint,
libraryOptions: *mut hipLibraryOption,
libraryOptionValues: *mut *mut ::std::os::raw::c_void,
numLibraryOptions: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLibraryLoadFromFile(
library: *mut hipLibrary_t,
fileName: *const ::std::os::raw::c_char,
jitOptions: *mut hipJitOption,
jitOptionsValues: *mut *mut ::std::os::raw::c_void,
numJitOptions: ::std::os::raw::c_uint,
libraryOptions: *mut hipLibraryOption,
libraryOptionValues: *mut *mut ::std::os::raw::c_void,
numLibraryOptions: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLibraryUnload(library: hipLibrary_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLibraryGetKernel(
pKernel: *mut hipKernel_t,
library: hipLibrary_t,
name: *const ::std::os::raw::c_char,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLibraryGetKernelCount(
count: *mut ::std::os::raw::c_uint,
library: hipLibrary_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipFuncGetAttributes(
attr: *mut hipFuncAttributes,
func: *const ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipFuncGetAttribute(
value: *mut ::std::os::raw::c_int,
attrib: hipFunction_attribute,
hfunc: hipFunction_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetFuncBySymbol(
functionPtr: *mut hipFunction_t,
symbolPtr: *const ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetDriverEntryPoint(
symbol: *const ::std::os::raw::c_char,
funcPtr: *mut *mut ::std::os::raw::c_void,
flags: ::std::os::raw::c_ulonglong,
driverStatus: *mut hipDriverEntryPointQueryResult,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleGetTexRef(
texRef: *mut *mut textureReference,
hmod: hipModule_t,
name: *const ::std::os::raw::c_char,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleLoadData(
module: *mut hipModule_t,
image: *const ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleLoadDataEx(
module: *mut hipModule_t,
image: *const ::std::os::raw::c_void,
numOptions: ::std::os::raw::c_uint,
options: *mut hipJitOption,
optionValues: *mut *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLinkAddData(
state: hipLinkState_t,
type_: hipJitInputType,
data: *mut ::std::os::raw::c_void,
size: usize,
name: *const ::std::os::raw::c_char,
numOptions: ::std::os::raw::c_uint,
options: *mut hipJitOption,
optionValues: *mut *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLinkAddFile(
state: hipLinkState_t,
type_: hipJitInputType,
path: *const ::std::os::raw::c_char,
numOptions: ::std::os::raw::c_uint,
options: *mut hipJitOption,
optionValues: *mut *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLinkComplete(
state: hipLinkState_t,
hipBinOut: *mut *mut ::std::os::raw::c_void,
sizeOut: *mut usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLinkCreate(
numOptions: ::std::os::raw::c_uint,
options: *mut hipJitOption,
optionValues: *mut *mut ::std::os::raw::c_void,
stateOut: *mut hipLinkState_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLinkDestroy(state: hipLinkState_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleLaunchKernel(
f: hipFunction_t,
gridDimX: ::std::os::raw::c_uint,
gridDimY: ::std::os::raw::c_uint,
gridDimZ: ::std::os::raw::c_uint,
blockDimX: ::std::os::raw::c_uint,
blockDimY: ::std::os::raw::c_uint,
blockDimZ: ::std::os::raw::c_uint,
sharedMemBytes: ::std::os::raw::c_uint,
stream: hipStream_t,
kernelParams: *mut *mut ::std::os::raw::c_void,
extra: *mut *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleLaunchCooperativeKernel(
f: hipFunction_t,
gridDimX: ::std::os::raw::c_uint,
gridDimY: ::std::os::raw::c_uint,
gridDimZ: ::std::os::raw::c_uint,
blockDimX: ::std::os::raw::c_uint,
blockDimY: ::std::os::raw::c_uint,
blockDimZ: ::std::os::raw::c_uint,
sharedMemBytes: ::std::os::raw::c_uint,
stream: hipStream_t,
kernelParams: *mut *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleLaunchCooperativeKernelMultiDevice(
launchParamsList: *mut hipFunctionLaunchParams,
numDevices: ::std::os::raw::c_uint,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLaunchCooperativeKernel(
f: *const ::std::os::raw::c_void,
gridDim: dim3,
blockDimX: dim3,
kernelParams: *mut *mut ::std::os::raw::c_void,
sharedMemBytes: ::std::os::raw::c_uint,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLaunchCooperativeKernelMultiDevice(
launchParamsList: *mut hipLaunchParams,
numDevices: ::std::os::raw::c_int,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipExtLaunchMultiKernelMultiDevice(
launchParamsList: *mut hipLaunchParams,
numDevices: ::std::os::raw::c_int,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLaunchKernelExC(
config: *const hipLaunchConfig_t,
fPtr: *const ::std::os::raw::c_void,
args: *mut *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvLaunchKernelEx(
config: *const HIP_LAUNCH_CONFIG,
f: hipFunction_t,
params: *mut *mut ::std::os::raw::c_void,
extra: *mut *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemGetHandleForAddressRange(
handle: *mut ::std::os::raw::c_void,
dptr: hipDeviceptr_t,
size: usize,
handleType: hipMemRangeHandleType,
flags: ::std::os::raw::c_ulonglong,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleOccupancyMaxPotentialBlockSize(
gridSize: *mut ::std::os::raw::c_int,
blockSize: *mut ::std::os::raw::c_int,
f: hipFunction_t,
dynSharedMemPerBlk: usize,
blockSizeLimit: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleOccupancyMaxPotentialBlockSizeWithFlags(
gridSize: *mut ::std::os::raw::c_int,
blockSize: *mut ::std::os::raw::c_int,
f: hipFunction_t,
dynSharedMemPerBlk: usize,
blockSizeLimit: ::std::os::raw::c_int,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleOccupancyMaxActiveBlocksPerMultiprocessor(
numBlocks: *mut ::std::os::raw::c_int,
f: hipFunction_t,
blockSize: ::std::os::raw::c_int,
dynSharedMemPerBlk: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipModuleOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(
numBlocks: *mut ::std::os::raw::c_int,
f: hipFunction_t,
blockSize: ::std::os::raw::c_int,
dynSharedMemPerBlk: usize,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipOccupancyMaxActiveBlocksPerMultiprocessor(
numBlocks: *mut ::std::os::raw::c_int,
f: *const ::std::os::raw::c_void,
blockSize: ::std::os::raw::c_int,
dynSharedMemPerBlk: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(
numBlocks: *mut ::std::os::raw::c_int,
f: *const ::std::os::raw::c_void,
blockSize: ::std::os::raw::c_int,
dynSharedMemPerBlk: usize,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipOccupancyMaxPotentialBlockSize(
gridSize: *mut ::std::os::raw::c_int,
blockSize: *mut ::std::os::raw::c_int,
f: *const ::std::os::raw::c_void,
dynSharedMemPerBlk: usize,
blockSizeLimit: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipProfilerStart() -> hipError_t;
}
unsafe extern "C" {
pub fn hipProfilerStop() -> hipError_t;
}
unsafe extern "C" {
pub fn hipConfigureCall(
gridDim: dim3,
blockDim: dim3,
sharedMem: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipSetupArgument(
arg: *const ::std::os::raw::c_void,
size: usize,
offset: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLaunchByPtr(func: *const ::std::os::raw::c_void) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLaunchKernel(
function_address: *const ::std::os::raw::c_void,
numBlocks: dim3,
dimBlocks: dim3,
args: *mut *mut ::std::os::raw::c_void,
sharedMemBytes: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLaunchHostFunc(
stream: hipStream_t,
fn_: hipHostFn_t,
userData: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvMemcpy2DUnaligned(pCopy: *const hip_Memcpy2D) -> hipError_t;
}
unsafe extern "C" {
pub fn hipExtLaunchKernel(
function_address: *const ::std::os::raw::c_void,
numBlocks: dim3,
dimBlocks: dim3,
args: *mut *mut ::std::os::raw::c_void,
sharedMemBytes: usize,
stream: hipStream_t,
startEvent: hipEvent_t,
stopEvent: hipEvent_t,
flags: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCreateTextureObject(
pTexObject: *mut hipTextureObject_t,
pResDesc: *const hipResourceDesc,
pTexDesc: *const hipTextureDesc,
pResViewDesc: *const hipResourceViewDesc,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDestroyTextureObject(textureObject: hipTextureObject_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetChannelDesc(
desc: *mut hipChannelFormatDesc,
array: hipArray_const_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetTextureObjectResourceDesc(
pResDesc: *mut hipResourceDesc,
textureObject: hipTextureObject_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetTextureObjectResourceViewDesc(
pResViewDesc: *mut hipResourceViewDesc,
textureObject: hipTextureObject_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetTextureObjectTextureDesc(
pTexDesc: *mut hipTextureDesc,
textureObject: hipTextureObject_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexObjectCreate(
pTexObject: *mut hipTextureObject_t,
pResDesc: *const HIP_RESOURCE_DESC,
pTexDesc: *const HIP_TEXTURE_DESC,
pResViewDesc: *const HIP_RESOURCE_VIEW_DESC,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexObjectDestroy(texObject: hipTextureObject_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexObjectGetResourceDesc(
pResDesc: *mut HIP_RESOURCE_DESC,
texObject: hipTextureObject_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexObjectGetResourceViewDesc(
pResViewDesc: *mut HIP_RESOURCE_VIEW_DESC,
texObject: hipTextureObject_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexObjectGetTextureDesc(
pTexDesc: *mut HIP_TEXTURE_DESC,
texObject: hipTextureObject_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMallocMipmappedArray(
mipmappedArray: *mut hipMipmappedArray_t,
desc: *const hipChannelFormatDesc,
extent: hipExtent,
numLevels: ::std::os::raw::c_uint,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipFreeMipmappedArray(mipmappedArray: hipMipmappedArray_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetMipmappedArrayLevel(
levelArray: *mut hipArray_t,
mipmappedArray: hipMipmappedArray_const_t,
level: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMipmappedArrayCreate(
pHandle: *mut hipMipmappedArray_t,
pMipmappedArrayDesc: *mut HIP_ARRAY3D_DESCRIPTOR,
numMipmapLevels: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMipmappedArrayDestroy(hMipmappedArray: hipMipmappedArray_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMipmappedArrayGetLevel(
pLevelArray: *mut hipArray_t,
hMipMappedArray: hipMipmappedArray_t,
level: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipBindTextureToMipmappedArray(
tex: *const textureReference,
mipmappedArray: hipMipmappedArray_const_t,
desc: *const hipChannelFormatDesc,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetTextureReference(
texref: *mut *const textureReference,
symbol: *const ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetBorderColor(
pBorderColor: *mut f32,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetArray(
pArray: *mut hipArray_t,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetAddressMode(
texRef: *mut textureReference,
dim: ::std::os::raw::c_int,
am: hipTextureAddressMode,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetArray(
tex: *mut textureReference,
array: hipArray_const_t,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetFilterMode(
texRef: *mut textureReference,
fm: hipTextureFilterMode,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetFlags(
texRef: *mut textureReference,
Flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetFormat(
texRef: *mut textureReference,
fmt: hipArray_Format,
NumPackedComponents: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipBindTexture(
offset: *mut usize,
tex: *const textureReference,
devPtr: *const ::std::os::raw::c_void,
desc: *const hipChannelFormatDesc,
size: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipBindTexture2D(
offset: *mut usize,
tex: *const textureReference,
devPtr: *const ::std::os::raw::c_void,
desc: *const hipChannelFormatDesc,
width: usize,
height: usize,
pitch: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipBindTextureToArray(
tex: *const textureReference,
array: hipArray_const_t,
desc: *const hipChannelFormatDesc,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetTextureAlignmentOffset(
offset: *mut usize,
texref: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipUnbindTexture(tex: *const textureReference) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetAddress(
dev_ptr: *mut hipDeviceptr_t,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetAddressMode(
pam: *mut hipTextureAddressMode,
texRef: *const textureReference,
dim: ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetFilterMode(
pfm: *mut hipTextureFilterMode,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetFlags(
pFlags: *mut ::std::os::raw::c_uint,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetFormat(
pFormat: *mut hipArray_Format,
pNumChannels: *mut ::std::os::raw::c_int,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetMaxAnisotropy(
pmaxAnsio: *mut ::std::os::raw::c_int,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetMipmapFilterMode(
pfm: *mut hipTextureFilterMode,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetMipmapLevelBias(
pbias: *mut f32,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetMipmapLevelClamp(
pminMipmapLevelClamp: *mut f32,
pmaxMipmapLevelClamp: *mut f32,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefGetMipMappedArray(
pArray: *mut hipMipmappedArray_t,
texRef: *const textureReference,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetAddress(
ByteOffset: *mut usize,
texRef: *mut textureReference,
dptr: hipDeviceptr_t,
bytes: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetAddress2D(
texRef: *mut textureReference,
desc: *const HIP_ARRAY_DESCRIPTOR,
dptr: hipDeviceptr_t,
Pitch: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetMaxAnisotropy(
texRef: *mut textureReference,
maxAniso: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetBorderColor(
texRef: *mut textureReference,
pBorderColor: *mut f32,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetMipmapFilterMode(
texRef: *mut textureReference,
fm: hipTextureFilterMode,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetMipmapLevelBias(texRef: *mut textureReference, bias: f32) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetMipmapLevelClamp(
texRef: *mut textureReference,
minMipMapLevelClamp: f32,
maxMipMapLevelClamp: f32,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipTexRefSetMipmappedArray(
texRef: *mut textureReference,
mipmappedArray: *mut hipMipmappedArray,
Flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipApiName(id: u32) -> *const ::std::os::raw::c_char;
}
unsafe extern "C" {
pub fn hipKernelNameRef(f: hipFunction_t) -> *const ::std::os::raw::c_char;
}
unsafe extern "C" {
pub fn hipKernelNameRefByPtr(
hostFunction: *const ::std::os::raw::c_void,
stream: hipStream_t,
) -> *const ::std::os::raw::c_char;
}
unsafe extern "C" {
pub fn hipGetStreamDeviceId(stream: hipStream_t) -> ::std::os::raw::c_int;
}
unsafe extern "C" {
pub fn hipStreamBeginCapture(stream: hipStream_t, mode: hipStreamCaptureMode) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamBeginCaptureToGraph(
stream: hipStream_t,
graph: hipGraph_t,
dependencies: *const hipGraphNode_t,
dependencyData: *const hipGraphEdgeData,
numDependencies: usize,
mode: hipStreamCaptureMode,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamEndCapture(stream: hipStream_t, pGraph: *mut hipGraph_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetCaptureInfo(
stream: hipStream_t,
pCaptureStatus: *mut hipStreamCaptureStatus,
pId: *mut ::std::os::raw::c_ulonglong,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetCaptureInfo_v2(
stream: hipStream_t,
captureStatus_out: *mut hipStreamCaptureStatus,
id_out: *mut ::std::os::raw::c_ulonglong,
graph_out: *mut hipGraph_t,
dependencies_out: *mut *const hipGraphNode_t,
numDependencies_out: *mut usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamIsCapturing(
stream: hipStream_t,
pCaptureStatus: *mut hipStreamCaptureStatus,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamUpdateCaptureDependencies(
stream: hipStream_t,
dependencies: *mut hipGraphNode_t,
numDependencies: usize,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipThreadExchangeStreamCaptureMode(mode: *mut hipStreamCaptureMode) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphCreate(pGraph: *mut hipGraph_t, flags: ::std::os::raw::c_uint) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphDestroy(graph: hipGraph_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddDependencies(
graph: hipGraph_t,
from: *const hipGraphNode_t,
to: *const hipGraphNode_t,
numDependencies: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphRemoveDependencies(
graph: hipGraph_t,
from: *const hipGraphNode_t,
to: *const hipGraphNode_t,
numDependencies: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphGetEdges(
graph: hipGraph_t,
from: *mut hipGraphNode_t,
to: *mut hipGraphNode_t,
numEdges: *mut usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphGetNodes(
graph: hipGraph_t,
nodes: *mut hipGraphNode_t,
numNodes: *mut usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphGetRootNodes(
graph: hipGraph_t,
pRootNodes: *mut hipGraphNode_t,
pNumRootNodes: *mut usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphNodeGetDependencies(
node: hipGraphNode_t,
pDependencies: *mut hipGraphNode_t,
pNumDependencies: *mut usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphNodeGetDependentNodes(
node: hipGraphNode_t,
pDependentNodes: *mut hipGraphNode_t,
pNumDependentNodes: *mut usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphNodeGetType(node: hipGraphNode_t, pType: *mut hipGraphNodeType) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphDestroyNode(node: hipGraphNode_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphClone(pGraphClone: *mut hipGraph_t, originalGraph: hipGraph_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphNodeFindInClone(
pNode: *mut hipGraphNode_t,
originalNode: hipGraphNode_t,
clonedGraph: hipGraph_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphInstantiate(
pGraphExec: *mut hipGraphExec_t,
graph: hipGraph_t,
pErrorNode: *mut hipGraphNode_t,
pLogBuffer: *mut ::std::os::raw::c_char,
bufferSize: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphInstantiateWithFlags(
pGraphExec: *mut hipGraphExec_t,
graph: hipGraph_t,
flags: ::std::os::raw::c_ulonglong,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphInstantiateWithParams(
pGraphExec: *mut hipGraphExec_t,
graph: hipGraph_t,
instantiateParams: *mut hipGraphInstantiateParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphLaunch(graphExec: hipGraphExec_t, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphUpload(graphExec: hipGraphExec_t, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
nodeParams: *mut hipGraphNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecGetFlags(
graphExec: hipGraphExec_t,
flags: *mut ::std::os::raw::c_ulonglong,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphNodeSetParams(
node: hipGraphNode_t,
nodeParams: *mut hipGraphNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecNodeSetParams(
graphExec: hipGraphExec_t,
node: hipGraphNode_t,
nodeParams: *mut hipGraphNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecDestroy(graphExec: hipGraphExec_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecUpdate(
hGraphExec: hipGraphExec_t,
hGraph: hipGraph_t,
hErrorNode_out: *mut hipGraphNode_t,
updateResult_out: *mut hipGraphExecUpdateResult,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddKernelNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
pNodeParams: *const hipKernelNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphKernelNodeGetParams(
node: hipGraphNode_t,
pNodeParams: *mut hipKernelNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphKernelNodeSetParams(
node: hipGraphNode_t,
pNodeParams: *const hipKernelNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecKernelNodeSetParams(
hGraphExec: hipGraphExec_t,
node: hipGraphNode_t,
pNodeParams: *const hipKernelNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvGraphAddMemcpyNode(
phGraphNode: *mut hipGraphNode_t,
hGraph: hipGraph_t,
dependencies: *const hipGraphNode_t,
numDependencies: usize,
copyParams: *const HIP_MEMCPY3D,
ctx: hipCtx_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddMemcpyNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
pCopyParams: *const hipMemcpy3DParms,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphMemcpyNodeGetParams(
node: hipGraphNode_t,
pNodeParams: *mut hipMemcpy3DParms,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphMemcpyNodeSetParams(
node: hipGraphNode_t,
pNodeParams: *const hipMemcpy3DParms,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphKernelNodeSetAttribute(
hNode: hipGraphNode_t,
attr: hipLaunchAttributeID,
value: *const hipLaunchAttributeValue,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphKernelNodeGetAttribute(
hNode: hipGraphNode_t,
attr: hipLaunchAttributeID,
value: *mut hipLaunchAttributeValue,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecMemcpyNodeSetParams(
hGraphExec: hipGraphExec_t,
node: hipGraphNode_t,
pNodeParams: *mut hipMemcpy3DParms,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddMemcpyNode1D(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
dst: *mut ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
count: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphMemcpyNodeSetParams1D(
node: hipGraphNode_t,
dst: *mut ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
count: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecMemcpyNodeSetParams1D(
hGraphExec: hipGraphExec_t,
node: hipGraphNode_t,
dst: *mut ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
count: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddMemcpyNodeFromSymbol(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
dst: *mut ::std::os::raw::c_void,
symbol: *const ::std::os::raw::c_void,
count: usize,
offset: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphMemcpyNodeSetParamsFromSymbol(
node: hipGraphNode_t,
dst: *mut ::std::os::raw::c_void,
symbol: *const ::std::os::raw::c_void,
count: usize,
offset: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecMemcpyNodeSetParamsFromSymbol(
hGraphExec: hipGraphExec_t,
node: hipGraphNode_t,
dst: *mut ::std::os::raw::c_void,
symbol: *const ::std::os::raw::c_void,
count: usize,
offset: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddMemcpyNodeToSymbol(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
symbol: *const ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
count: usize,
offset: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphMemcpyNodeSetParamsToSymbol(
node: hipGraphNode_t,
symbol: *const ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
count: usize,
offset: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecMemcpyNodeSetParamsToSymbol(
hGraphExec: hipGraphExec_t,
node: hipGraphNode_t,
symbol: *const ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
count: usize,
offset: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddMemsetNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
pMemsetParams: *const hipMemsetParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphMemsetNodeGetParams(
node: hipGraphNode_t,
pNodeParams: *mut hipMemsetParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphMemsetNodeSetParams(
node: hipGraphNode_t,
pNodeParams: *const hipMemsetParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecMemsetNodeSetParams(
hGraphExec: hipGraphExec_t,
node: hipGraphNode_t,
pNodeParams: *const hipMemsetParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddHostNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
pNodeParams: *const hipHostNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphHostNodeGetParams(
node: hipGraphNode_t,
pNodeParams: *mut hipHostNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphHostNodeSetParams(
node: hipGraphNode_t,
pNodeParams: *const hipHostNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecHostNodeSetParams(
hGraphExec: hipGraphExec_t,
node: hipGraphNode_t,
pNodeParams: *const hipHostNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddChildGraphNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
childGraph: hipGraph_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphChildGraphNodeGetGraph(
node: hipGraphNode_t,
pGraph: *mut hipGraph_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecChildGraphNodeSetParams(
hGraphExec: hipGraphExec_t,
node: hipGraphNode_t,
childGraph: hipGraph_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddEmptyNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddEventRecordNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
event: hipEvent_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphEventRecordNodeGetEvent(
node: hipGraphNode_t,
event_out: *mut hipEvent_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphEventRecordNodeSetEvent(node: hipGraphNode_t, event: hipEvent_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecEventRecordNodeSetEvent(
hGraphExec: hipGraphExec_t,
hNode: hipGraphNode_t,
event: hipEvent_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddEventWaitNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
event: hipEvent_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphEventWaitNodeGetEvent(
node: hipGraphNode_t,
event_out: *mut hipEvent_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphEventWaitNodeSetEvent(node: hipGraphNode_t, event: hipEvent_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecEventWaitNodeSetEvent(
hGraphExec: hipGraphExec_t,
hNode: hipGraphNode_t,
event: hipEvent_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddMemAllocNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
pNodeParams: *mut hipMemAllocNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphMemAllocNodeGetParams(
node: hipGraphNode_t,
pNodeParams: *mut hipMemAllocNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddMemFreeNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
dev_ptr: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphMemFreeNodeGetParams(
node: hipGraphNode_t,
dev_ptr: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGetGraphMemAttribute(
device: ::std::os::raw::c_int,
attr: hipGraphMemAttributeType,
value: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceSetGraphMemAttribute(
device: ::std::os::raw::c_int,
attr: hipGraphMemAttributeType,
value: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDeviceGraphMemTrim(device: ::std::os::raw::c_int) -> hipError_t;
}
unsafe extern "C" {
pub fn hipUserObjectCreate(
object_out: *mut hipUserObject_t,
ptr: *mut ::std::os::raw::c_void,
destroy: hipHostFn_t,
initialRefcount: ::std::os::raw::c_uint,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipUserObjectRelease(
object: hipUserObject_t,
count: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipUserObjectRetain(
object: hipUserObject_t,
count: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphRetainUserObject(
graph: hipGraph_t,
object: hipUserObject_t,
count: ::std::os::raw::c_uint,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphReleaseUserObject(
graph: hipGraph_t,
object: hipUserObject_t,
count: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphDebugDotPrint(
graph: hipGraph_t,
path: *const ::std::os::raw::c_char,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphKernelNodeCopyAttributes(
hSrc: hipGraphNode_t,
hDst: hipGraphNode_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphNodeSetEnabled(
hGraphExec: hipGraphExec_t,
hNode: hipGraphNode_t,
isEnabled: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphNodeGetEnabled(
hGraphExec: hipGraphExec_t,
hNode: hipGraphNode_t,
isEnabled: *mut ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddExternalSemaphoresWaitNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
nodeParams: *const hipExternalSemaphoreWaitNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphAddExternalSemaphoresSignalNode(
pGraphNode: *mut hipGraphNode_t,
graph: hipGraph_t,
pDependencies: *const hipGraphNode_t,
numDependencies: usize,
nodeParams: *const hipExternalSemaphoreSignalNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExternalSemaphoresSignalNodeSetParams(
hNode: hipGraphNode_t,
nodeParams: *const hipExternalSemaphoreSignalNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExternalSemaphoresWaitNodeSetParams(
hNode: hipGraphNode_t,
nodeParams: *const hipExternalSemaphoreWaitNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExternalSemaphoresSignalNodeGetParams(
hNode: hipGraphNode_t,
params_out: *mut hipExternalSemaphoreSignalNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExternalSemaphoresWaitNodeGetParams(
hNode: hipGraphNode_t,
params_out: *mut hipExternalSemaphoreWaitNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecExternalSemaphoresSignalNodeSetParams(
hGraphExec: hipGraphExec_t,
hNode: hipGraphNode_t,
nodeParams: *const hipExternalSemaphoreSignalNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphExecExternalSemaphoresWaitNodeSetParams(
hGraphExec: hipGraphExec_t,
hNode: hipGraphNode_t,
nodeParams: *const hipExternalSemaphoreWaitNodeParams,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvGraphMemcpyNodeGetParams(
hNode: hipGraphNode_t,
nodeParams: *mut HIP_MEMCPY3D,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvGraphMemcpyNodeSetParams(
hNode: hipGraphNode_t,
nodeParams: *const HIP_MEMCPY3D,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvGraphAddMemsetNode(
phGraphNode: *mut hipGraphNode_t,
hGraph: hipGraph_t,
dependencies: *const hipGraphNode_t,
numDependencies: usize,
memsetParams: *const hipMemsetParams,
ctx: hipCtx_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvGraphAddMemFreeNode(
phGraphNode: *mut hipGraphNode_t,
hGraph: hipGraph_t,
dependencies: *const hipGraphNode_t,
numDependencies: usize,
dptr: hipDeviceptr_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvGraphExecMemcpyNodeSetParams(
hGraphExec: hipGraphExec_t,
hNode: hipGraphNode_t,
copyParams: *const HIP_MEMCPY3D,
ctx: hipCtx_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDrvGraphExecMemsetNodeSetParams(
hGraphExec: hipGraphExec_t,
hNode: hipGraphNode_t,
memsetParams: *const hipMemsetParams,
ctx: hipCtx_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemAddressFree(devPtr: *mut ::std::os::raw::c_void, size: usize) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemAddressReserve(
ptr: *mut *mut ::std::os::raw::c_void,
size: usize,
alignment: usize,
addr: *mut ::std::os::raw::c_void,
flags: ::std::os::raw::c_ulonglong,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemCreate(
handle: *mut hipMemGenericAllocationHandle_t,
size: usize,
prop: *const hipMemAllocationProp,
flags: ::std::os::raw::c_ulonglong,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemExportToShareableHandle(
shareableHandle: *mut ::std::os::raw::c_void,
handle: hipMemGenericAllocationHandle_t,
handleType: hipMemAllocationHandleType,
flags: ::std::os::raw::c_ulonglong,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemGetAccess(
flags: *mut ::std::os::raw::c_ulonglong,
location: *const hipMemLocation,
ptr: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemGetAllocationGranularity(
granularity: *mut usize,
prop: *const hipMemAllocationProp,
option: hipMemAllocationGranularity_flags,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemGetAllocationPropertiesFromHandle(
prop: *mut hipMemAllocationProp,
handle: hipMemGenericAllocationHandle_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemImportFromShareableHandle(
handle: *mut hipMemGenericAllocationHandle_t,
osHandle: *mut ::std::os::raw::c_void,
shHandleType: hipMemAllocationHandleType,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemMap(
ptr: *mut ::std::os::raw::c_void,
size: usize,
offset: usize,
handle: hipMemGenericAllocationHandle_t,
flags: ::std::os::raw::c_ulonglong,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemMapArrayAsync(
mapInfoList: *mut hipArrayMapInfo,
count: ::std::os::raw::c_uint,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemRelease(handle: hipMemGenericAllocationHandle_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemRetainAllocationHandle(
handle: *mut hipMemGenericAllocationHandle_t,
addr: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemSetAccess(
ptr: *mut ::std::os::raw::c_void,
size: usize,
desc: *const hipMemAccessDesc,
count: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemUnmap(ptr: *mut ::std::os::raw::c_void, size: usize) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphicsMapResources(
count: ::std::os::raw::c_int,
resources: *mut hipGraphicsResource_t,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphicsSubResourceGetMappedArray(
array: *mut hipArray_t,
resource: hipGraphicsResource_t,
arrayIndex: ::std::os::raw::c_uint,
mipLevel: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphicsResourceGetMappedPointer(
devPtr: *mut *mut ::std::os::raw::c_void,
size: *mut usize,
resource: hipGraphicsResource_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphicsUnmapResources(
count: ::std::os::raw::c_int,
resources: *mut hipGraphicsResource_t,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphicsUnregisterResource(resource: hipGraphicsResource_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipCreateSurfaceObject(
pSurfObject: *mut hipSurfaceObject_t,
pResDesc: *const hipResourceDesc,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipDestroySurfaceObject(surfaceObject: hipSurfaceObject_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy_spt(
dst: *mut ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyToSymbol_spt(
symbol: *const ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
offset: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyFromSymbol_spt(
dst: *mut ::std::os::raw::c_void,
symbol: *const ::std::os::raw::c_void,
sizeBytes: usize,
offset: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2D_spt(
dst: *mut ::std::os::raw::c_void,
dpitch: usize,
src: *const ::std::os::raw::c_void,
spitch: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DFromArray_spt(
dst: *mut ::std::os::raw::c_void,
dpitch: usize,
src: hipArray_const_t,
wOffset: usize,
hOffset: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy3D_spt(p: *const hipMemcpy3DParms) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemset_spt(
dst: *mut ::std::os::raw::c_void,
value: ::std::os::raw::c_int,
sizeBytes: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemsetAsync_spt(
dst: *mut ::std::os::raw::c_void,
value: ::std::os::raw::c_int,
sizeBytes: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemset2D_spt(
dst: *mut ::std::os::raw::c_void,
pitch: usize,
value: ::std::os::raw::c_int,
width: usize,
height: usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemset2DAsync_spt(
dst: *mut ::std::os::raw::c_void,
pitch: usize,
value: ::std::os::raw::c_int,
width: usize,
height: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemset3DAsync_spt(
pitchedDevPtr: hipPitchedPtr,
value: ::std::os::raw::c_int,
extent: hipExtent,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemset3D_spt(
pitchedDevPtr: hipPitchedPtr,
value: ::std::os::raw::c_int,
extent: hipExtent,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyAsync_spt(
dst: *mut ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy3DAsync_spt(p: *const hipMemcpy3DParms, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DAsync_spt(
dst: *mut ::std::os::raw::c_void,
dpitch: usize,
src: *const ::std::os::raw::c_void,
spitch: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyFromSymbolAsync_spt(
dst: *mut ::std::os::raw::c_void,
symbol: *const ::std::os::raw::c_void,
sizeBytes: usize,
offset: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyToSymbolAsync_spt(
symbol: *const ::std::os::raw::c_void,
src: *const ::std::os::raw::c_void,
sizeBytes: usize,
offset: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpyFromArray_spt(
dst: *mut ::std::os::raw::c_void,
src: hipArray_const_t,
wOffsetSrc: usize,
hOffset: usize,
count: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DToArray_spt(
dst: hipArray_t,
wOffset: usize,
hOffset: usize,
src: *const ::std::os::raw::c_void,
spitch: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DFromArrayAsync_spt(
dst: *mut ::std::os::raw::c_void,
dpitch: usize,
src: hipArray_const_t,
wOffsetSrc: usize,
hOffsetSrc: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipMemcpy2DToArrayAsync_spt(
dst: hipArray_t,
wOffset: usize,
hOffset: usize,
src: *const ::std::os::raw::c_void,
spitch: usize,
width: usize,
height: usize,
kind: hipMemcpyKind,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamQuery_spt(stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamSynchronize_spt(stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetPriority_spt(
stream: hipStream_t,
priority: *mut ::std::os::raw::c_int,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamWaitEvent_spt(
stream: hipStream_t,
event: hipEvent_t,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetFlags_spt(
stream: hipStream_t,
flags: *mut ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamAddCallback_spt(
stream: hipStream_t,
callback: hipStreamCallback_t,
userData: *mut ::std::os::raw::c_void,
flags: ::std::os::raw::c_uint,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipEventRecord_spt(event: hipEvent_t, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLaunchCooperativeKernel_spt(
f: *const ::std::os::raw::c_void,
gridDim: dim3,
blockDim: dim3,
kernelParams: *mut *mut ::std::os::raw::c_void,
sharedMemBytes: u32,
hStream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLaunchKernel_spt(
function_address: *const ::std::os::raw::c_void,
numBlocks: dim3,
dimBlocks: dim3,
args: *mut *mut ::std::os::raw::c_void,
sharedMemBytes: usize,
stream: hipStream_t,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGraphLaunch_spt(graphExec: hipGraphExec_t, stream: hipStream_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamBeginCapture_spt(stream: hipStream_t, mode: hipStreamCaptureMode)
-> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamEndCapture_spt(stream: hipStream_t, pGraph: *mut hipGraph_t) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamIsCapturing_spt(
stream: hipStream_t,
pCaptureStatus: *mut hipStreamCaptureStatus,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetCaptureInfo_spt(
stream: hipStream_t,
pCaptureStatus: *mut hipStreamCaptureStatus,
pId: *mut ::std::os::raw::c_ulonglong,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipStreamGetCaptureInfo_v2_spt(
stream: hipStream_t,
captureStatus_out: *mut hipStreamCaptureStatus,
id_out: *mut ::std::os::raw::c_ulonglong,
graph_out: *mut hipGraph_t,
dependencies_out: *mut *const hipGraphNode_t,
numDependencies_out: *mut usize,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipLaunchHostFunc_spt(
stream: hipStream_t,
fn_: hipHostFn_t,
userData: *mut ::std::os::raw::c_void,
) -> hipError_t;
}
unsafe extern "C" {
pub fn hipGetDriverEntryPoint_spt(
symbol: *const ::std::os::raw::c_char,
funcPtr: *mut *mut ::std::os::raw::c_void,
flags: ::std::os::raw::c_ulonglong,
status: *mut hipDriverEntryPointQueryResult,
) -> hipError_t;
}