CUDA가 예상대로 작동하지 않습니까?

Question

나는 CUDA 코드를 프로그래밍했다.

unsigned long mask_buffer; 
int s; 
off_t p, 

for(p=0;p!=5000;p++) 
{ 
    for(s=start;s!=end;s++) 
    { 
     ref_off = *(((unsigned int*)(idx_base)) + p); 

     if((int)(first_indexes[s-start_sequence] % 8 - ref_off % 8) < 0) 
     { 
      int shamt2 = (ref_off % 8 - first_indexes[s-start_sequence] % 8); 
      mask_buffer = *((unsigned long *)(msk_base + (ref_off - first_indexes[s-start_sequence])/8)) >> shamt2; 

      if(((*(unsigned long *)(seqmaskc + 16 * (s-start_sequence)))^mask_buffer) << shamt2) 
       continue; 
     } 

     else if((int)(first_indexes[s-start_sequence] % 8 - ref_off % 8) == 0) 
     { 
      mask_buffer = *((unsigned long *)(msk_base + (ref_off)/8)); 

      if((*(unsigned long *)(seqmaskc + 16 * (s-start_sequence))^mask_buffer)) 
       continue; 
     } 

     else 
     { 
      int shamt2 = 8 - (first_indexes[s-start_sequence] % 8 - ref_off % 8); 
      mask_buffer = *((unsigned long *)(msk_base + (ref_off/8- first_indexes[s-start_sequence]/8) - 1)) >> shamt2; 

      if(((*(unsigned long *)(seqmaskc + 16 * (s-start_sequence)))^mask_buffer) << shamt2) 
       continue; 
     } 

     int shamt = (ref_off % 4 - first_indexes[s-start_sequence] % 4) * 2; 

     memcpy(reference_blk, ref_base + ref_off/4 - first_indexes[s-start_sequence]/4, sequence_bytes); 

     for (rp = last_rp ; rp != (unsigned long *) reference_blk ; rp--) 
     { 
      unsigned long tmp = ((*rp) & ((1 << shamt) - 1)) << (8 * sizeof(unsigned long) - shamt); 
      *rp = (*rp >> shamt) | shifted_in; 
      shifted_in = tmp; 
     } 

     *rp = (*rp >> shamt) | shifted_in; 

     if (sequence_length & 0x3) 
      reference_blk[sequence_length >> 2] &= (1 << ((sequence_length & 0x3) << 1)) - 1; 

     for (i = sequence_length >> 2 ; i & (SEQUENCE_ALIGN - 1) ; i++) 
      reference_blk[i] = 0; 

     //-- instead of memcmp --// 
     int v = 0; 
     char *p1 = (char *)sequence; 
     char *p2 = (char *)reference_blk; 
     int tmp_asd = sequence_bytes; 

     while(tmp_asd!=0) 
     { 
      v = *(p1++) - *(p2++); 

      if(v!=0) 
       break; 

      tmp_asd--; 
     } 

     if(v == 0) 
     { 
      mat_count[s - (int)start_sequence]++;  /* Maintain count */ 
      mat_position[s - (int)start_sequence] = ref_off-first_indexes[s-start_sequence]; /* Record latest position */ 
     } 

    } 
} 

이 for 루프는 내 코드의 주요 기능입니다. 그러나 문제는 변수 "p"가 5 또는 6 이상으로 증가하지 않는다는 것입니다. 내 컴퓨터에 GT530이 있고 내 CUDA 드라이버 버전과 런타임 버전도 4.0입니다. 이 코드의 문제점은 무엇입니까 ???

Answer 1

실제로 이것이 새로운 코드 편집 이전에 게시 된 원래의 커널이라고 가정하면 memcpy과 같은 표준 C 라이브러리 함수를 CUDA 커널 안에 호출 할 수 없습니다. 코드). 커널에서는 __device__ 기능 만 호출 할 수 있습니다. 따라서 CUDA에서 memcpy을 다시 구현하지 않는 한, 커널 내부에서 그 함수를 호출하면 작동하지 않습니다 ...

또한 결과를 확인해야하는 CUDA 커널을 작성하려고한다면 커널의 메모리 비교 섹션에서 수행하는 것처럼 그룹의 다른 스레드가 작성한 것보다 코드에 동기화 지점을 추가하여 모든 스레드가 특정 지점에 도달했는지 확인해야합니다 해당 스레드의 결과를 확인하기 시작하십시오. 또 다른 블록이 주 메모리에 기록되었을 수있는 내용을 확인하려는 경우 이전 주 스레드 블록의 결과가 주 메모리에 기록되도록 보장하는 동기화 기본도 있습니다.