CUDA 상수 메모리 값이 잘못되었습니다.

Question

상수 메모리와 관련된 많은 SO 질문을 읽었으므로 왜 프로그램이 작동하지 않는지 아직 이해할 수 없습니다.

Common.cuh

__constant__ int numElements; 

__global__ 
void kernelFunction(); 

Common.cu

#include "Common.cuh" 
#include <stdio.h> 

__global__ 
kernelFunction() 
{ 
    printf("NumElements = %d", numElements); 
} 

Test.cu

#include "Common.cuh" 

int main() 
{ 
    int N = 100; 
    cudaMemcpyToSymbol(numElements,&N,sizeof(int)); 
    kernelFunction<<<1,1>>>(); 
    cudaDeviceSynchronize(); 
    return 0; 
} 

I을 다음과 같이 전체적으로 본다 t는 오류없이 컴파일하지만 numElements 값을 인쇄 할 때 나는 임의의 값을 얻는다. 누군가가 이것을 이해할 수있는 올바른 방향으로 나를 가리킬 수 있습니까?

Answer 1

이 라인 :

__constant__ int numElements; 

는 컴파일 부 범위를 갖는다. 즉, 하나의 모듈과 다른 모듈로 컴파일하면 numElements의 __constant__ 메모리에 서로 다른 인스턴스가 생성됩니다.

해결 방법은 두 개의 모듈을 함께 장치 링크하기 위해 separate compilation and linking을 사용하는 것입니다. 이때 장치 링커가 두 모듈간에 기호를 확인합니다.

nvcc -arch=sm_20 -rdc=true -o test common.cu test.cu 

예 : 전용 ** Common.cu ** 상수 변수`numElements`을 사용하는 경우

$ cat common.cuh 
#ifndef COMMON_CU 
extern __constant__ int numElements; 
#endif 
__global__ 
void kernelFunction(); 
$ cat common.cu 
#define COMMON_CU 
#include "common.cuh" 
#include <stdio.h> 

__constant__ int numElements; 
__global__ 
void kernelFunction() 
{ 
    printf("NumElements = %d\n", numElements); 
} 
$ cat test.cu 
#define TEST_CU 
#include "common.cuh" 

int main() 
{ 
    int N = 100; 
    cudaMemcpyToSymbol(numElements,&N,sizeof(int)); 
    kernelFunction<<<1,1>>>(); 
    cudaDeviceSynchronize(); 
    return 0; 
} 

$ nvcc -arch=sm_20 -rdc=true -o test common.cu test.cu 
$ ./test 
NumElements = 100 
$