mirrors/ZLUDA
0
0
Fork 0
mirror of https://github.com/vosen/ZLUDA.git synced 2025-09-27 03:39:10 +00:00
Code Issues Projects Releases Packages Wiki Activity Actions 2

Avoid memset in malloc during capturing

Browse source
This commit is contained in:
Andrzej Janik 2025-09-25 22:44:49 +00:00
commit a8fa8089c0
1 changed files with 10 additions and 7 deletions
Download patch file Download diff file Expand all files Collapse all files

17
zluda/src/impl/memory.rs
View file

@ -1,16 +1,18 @@
use std::ptr;
use crate::r#impl::{context, driver};
use cuda_types::cuda::{CUerror, CUresult, CUresultConsts};
use hip_runtime_sys::*;
use std::{mem, ptr};
use crate::r#impl::{context, driver};
pub(crate) fn alloc_v2(dptr: &mut hipDeviceptr_t, bytesize: usize) -> CUresult {
pub(crate) unsafe fn alloc_v2(dptr: &mut hipDeviceptr_t, bytesize: usize) -> CUresult {
let context = context::get_current_context()?;
unsafe { hipMalloc(ptr::from_mut(dptr).cast(), bytesize) }?;
hipMalloc(ptr::from_mut(dptr).cast(), bytesize)?;
add_allocation(dptr.0, bytesize, context)?;
let mut status = mem::zeroed();
hipStreamIsCapturing(hipStream_t(ptr::null_mut()), &mut status)?;
// TODO: parametrize for non-Geekbench
unsafe { hipMemsetD8(*dptr, 0, bytesize) }?;
if status != hipStreamCaptureStatus::hipStreamCaptureStatusNone {
hipMemsetD8(*dptr, 0, bytesize)?;
}
Ok(())
}
@ -68,6 +70,7 @@ pub(crate) unsafe fn host_alloc(
) -> CUresult {
let context = context::get_current_context()?;
hipHostMalloc(pp, bytesize, flags)?;
unsafe { hipMemsetD8(hipDeviceptr_t(*pp), 0, bytesize) }?;
add_allocation(*pp, bytesize, context)?;
Ok(())
}