Difference between host cudaMalloc() and kernel malloc()

Accelerated Computing CUDA CUDA Programming and Performance
#1

The programmer’s manual say that the host cudaMalloc() are automatically aligned to 256 bytes. This might result in wastage of memory if the allocated memory size is small.

the driver or runtime API is always aligned to at least 256 bytes (CUDA 4.0 Manual Page 95)

But the kernel side malloc() calls are aligned to 16 bytes.

The returned pointer is guaranteed to be aligned to a 16-byte boundary (CUDA 4.0 Manual Page 126/Dynamic Global memory allocation)

Anyone knows why this difference ?

#2

I don’t know, but I can imagine that kernel side malloc() is expected to be used for smaller chunks of memory, so the balance got shifted to their favor.