Skip to content

Commit abbd1ec

Browse files
committed
cuBLAS: do not use pinned memory if env variable GGML_CUDA_NO_PINNED is set
1 parent 576a3bd commit abbd1ec

File tree

1 file changed

+5
-2
lines changed

1 file changed

+5
-2
lines changed

ggml-cuda.cu

Lines changed: 5 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -355,13 +355,16 @@ cudaError_t ggml_cuda_h2d_tensor_2d(void * dst, const struct ggml_tensor * src,
355355
}
356356

357357
void * ggml_cuda_host_malloc(size_t size) {
358-
void * ptr = nullptr;
358+
if (getenv("GGML_CUDA_NO_PINNED") != nullptr) {
359+
return nullptr;
360+
}
359361

362+
void * ptr = nullptr;
360363
cudaError_t err = cudaMallocHost((void **) &ptr, size);
361364
if (err != cudaSuccess) {
362365
fprintf(stderr, "WARNING: failed to allocate %.2f MB of pinned memory: %s\n",
363366
size/1024.0/1024.0, cudaGetErrorString(err));
364-
return NULL;
367+
return nullptr;
365368
}
366369

367370
return ptr;

0 commit comments

Comments
 (0)