CUDA에서 배열의 요소를 지정하기

Question

CUDA에서 병렬 프로그래밍으로 배열의 요소 (행렬)를 변경해야합니다.

내 시도는 위의 방법이 작동하지 않는 다음

__global__ void CudaProcessingKernel(int *dataA) 
{ 

    int bx = blockIdx.x; 
    int tx = threadIdx.x; 
    int tid = bx * XTHREADS + tx; 

    if(tid< 16)  // matrix 4x4 
    { 

     if(tid==4) dataB[tid]=dataB[5]; 
     if(tid==5) dataB[tid]=dataB[6]; 
     if(tid==6) dataB[tid]=dataB[7]; 
     if(tid==7) dataB[tid]=dataB[4]; 
    } 

    __syncthreads(); 
}   

입니다.

내가 원하는 것은 :

input B[1][] = **EC 6E 4C 90** => output **6E 4C 90 EC** 

내 출력은 다음과 같습니다

**6E 90 4C 6E** 

B[4] 및 B[7]가 같은 값을 가지고있다. 병렬 처리의 경우, 임시 저장 영역을 피할 수 있어야한다고 생각합니다 : int TEMP = B[4]; B[7]=TEMP.

내 잘못이 무엇입니까? 어떤 종류의 기억을 사용해야합니까?

Answer 1

나는 원자력 작전을 사용하여 당신이 관찰하고있는 경쟁 조건을 피하기 위해 제안합니다. 원자 적 연산으로 atomicCAS을 사용할 수 있습니다. 아래의 접근 방식은 모든 그리드 크기에서 작동합니다. 다른 방법으로, 임시 배열 (게시물에서 언급했듯이)을 정의하고 원자 적 연산을 피할 수 있습니다.

다음은 CUDA 아토믹을 사용하는 코드입니다.

#include <stdio.h> 

#define N 10 

__global__ void swap_kernel(int* data) { 

    int tid = blockIdx.x*blockDim.x + threadIdx.x; 

    if (tid < N) { atomicCAS(&data[tid], data[tid], data[(tid+1) % N]); } 

} 

void main() { 

    int* h_vec = (int*) malloc(N*sizeof(int)); 
    int* d_vec; cudaMalloc((void**)&d_vec,N*sizeof(int)); 

    for (int i=0; i<N; i++) h_vec[i] = i; 

    cudaMemcpy(d_vec,h_vec,N*sizeof(int),cudaMemcpyHostToDevice); 

    swap_kernel<<<2,8>>>(d_vec); 

    cudaMemcpy(h_vec,d_vec,N*sizeof(int),cudaMemcpyDeviceToHost); 

    for (int i=0; i<N; i++) printf("%i %i\n",i,h_vec[i]); 

    getchar(); 

} 

Answer 2

다른 사람이 읽는 동안 출력이 틀리도록 전역에서 데이터를 수정하고 있습니다. 너는 그런 식으로해야한다. 데이터를 읽은 것처럼 모든 스레드에 등록 된 데이터가 있으면 배열의 새 요소에 쓰게됩니다. 좋아요 :