CUDA 스레드로 전역 메모리 복사

Question

전역 메모리의 한 배열을 CUDA 스레드 (호스트가 아닌)가 전역 메모리의 다른 배열에 복사해야합니다. 다음과 같이

내 코드는 다음과 같습니다

이

__global__ void copy_kernel(int *g_data1, int *g_data2, int n) 
{ 
    int idx = blockIdx.x * blockDim.x + threadIdx.x; 
    int start, end; 
    start = some_func(idx); 
    end = another_func(idx); 
    unsigned int i; 
    for (i = start; i < end; i++) { 
     g_data2[i] = g_data1[idx]; 
    } 
} 

이 때문에 일부 IDX 매우 비효율적이다, [시작, 종료] 지역 스레드의 문제가 너무 많은 복사 명령을 만드는 매우 크다. 효율적으로 구현할 수있는 방법이 있습니까?

는

청이 사용

Answer 1

시도 감사 :

CUresult cuMemcpyDtoD(
    CUdeviceptr dst, 
    CUdeviceptr src, 
    unsigned int bytes 
) 

UPDATE :

당신 맞아요 : http://forums.nvidia.com/index.php?showtopic=88745

이 할 수있는 더 효율적인 방법이 없습니다 이것은 CUDA의 설계가 당신이 오직 sm 커널의 모든 데이터 양.

Answer 2

당신이 작성한 방식대로 각 스레드가 '끝'청크에 전체 '시작'을 쓰려고합니다. 실제로 은 실제로 비효율적입니다.

이와 같이해야합니다.

___shared___ unsigned sm_start[BLOCK_SIZE]; 
___shared___ unsigned sm_end[BLOCK_SIZE]; 
sm_start[threadIdx.x] = start; 
sm_end[threadIdx.y] = end; 
__syncthreads(); 
for (int n = 0; n < blockdDim.x; n++) { 
g_data2 += sm_start[n]; 
unsigned lim = sm_end[n] - sm_start[n]; 
    for (int i = threadIdx.x; i < lim; i += blockDim.x) { 
     g_data2[i] = g_data1[idx]; 
    } 
}