Last active
September 2, 2019 02:39
-
-
Save sonots/41daaa6432b1c8b27ef782cd14064269 to your computer and use it in GitHub Desktop.
invetigation on cudaMalloc alignment => aligned to at least **512** bytes
This file contains hidden or bidirectional Unicode text that may be interpreted or compiled differently than what appears below. To review, open the file in an editor that reveals hidden Unicode characters.
Learn more about bidirectional Unicode characters
| #include <sys/time.h> | |
| #include <cuda_runtime.h> | |
| #include <stdio.h> | |
| void test(int size) | |
| { | |
| float *d1, *d2; | |
| cudaMalloc(&d1, size); | |
| cudaMalloc(&d2, size); | |
| printf("Alignment: %ld\n", (d2 - d1) * sizeof(float)); | |
| cudaFree(d1); | |
| cudaFree(d2); | |
| } | |
| int main(int argc, char **argv) | |
| { | |
| // set up device | |
| int dev = 0; | |
| cudaDeviceProp deviceProp; | |
| cudaGetDeviceProperties(&deviceProp, dev); | |
| printf("Using Device %d: %s\n", dev, deviceProp.name); | |
| cudaSetDevice(dev); | |
| test(1); | |
| return(0); | |
| } |
Sign up for free
to join this conversation on GitHub.
Already have an account?
Sign in to comment
I was also looking into this property, and my theory for the 512 bytes alignment is that the device pointer returned by
cudaMalloccould be used to back the texture memory, which requires the data to be aligned totextureAlignment(=512 bytes on V100). See, e.g., thecudaResourceDescsession in CUDA Runtime API.