I successfully set the cudaLimitStackSize to 124KB using cudaDeviceSetLimit, and afterwards was able to define a large enough array in the kernel function. However, when I attempted to restore cudaLimitStackSize by setting it to 1KB using cudaDeviceSetLimit, the kernel function that was previously w…

LOCAL MEMORY ALLOCATION On existing GPUs increasing the per thread stack size (cudaLimitStackSize) results in increasing the local memory allocation to RoundToAllocationGranularity(requestedSize) * CU_DEVICE_ATTRIBUTE_MULTIPROCESSOR_COUNT * CU_DEVICE_ATTRIBUTE_MAX_THREADS_PER_MULTIPROCESSOR. On a …

Not sure, whether it is possible to later on change the stack size. You could make your kernel a template function (or declare and define two copies with different names of the kernel) to have several copies of it and set the individual stack sizes.

size_t myStackSize = 124.5 * 1024; cudaError_t stat = cudaDeviceSetLimit (cudaLimitStackSize, myStackSize); assert(stat == 0); stat = cudaDeviceGetLimit (&myStackSize, cudaLimitStackSize); assert(stat == 0); printf("%zu", myStackSize); ... __global__ void kernelFunc(.....) { uint64_t array[159…

Can you run the kernel first and then set a stack size limit? Under the assumption, once the kernel was run, you cannot change the stack size.

cudaDeviceSetLimit bug

Accelerated Computing CUDA CUDA Programming and Performance

Robert_Crovella January 21, 2025, 12:49pm 5

this may be of interest

Topic		Replies	Views
cudaDeviceSetLimit call increases the GPU memory CUDA Programming and Performance	2	1168	September 28, 2016
How CUDA driver set stack size on kernel invocation? CUDA Programming and Performance	0	1202	May 21, 2019
What is the maximum CUDA Stack frame size per Kerenl. CUDA Programming and Performance	1	13779	November 18, 2013
Set stack size limit not working CUDA Programming and Performance	1	949	October 31, 2014
Maximum stack size? CUDA Programming and Performance	7	1499	March 24, 2024
show sizes of GPU memory usage, eg log cudaMalloc, CUDA reports "out of memory" at runtime CUDA Programming and Performance	4	2212	December 13, 2016
CUDA thread local array memory is not released after finished kernel execution CUDA Programming and Performance	2	1428	December 1, 2019
invalid argument error while using cudaDeviceSetLimit in cuda kernel CUDA Programming and Performance	3	2322	August 15, 2014
Recursion Depth on C2050? CUDA Programming and Performance	6	1929	August 23, 2010
hardware stack error? CUDA Programming and Performance	2	4306	May 18, 2016

cudaDeviceSetLimit bug

Related topics