CUDA는 CUDA CI를 사용

Question

을 실행하지 않는 커널의 원인 부동의 혼합을 두 번하는 것은 통계 커널을 그 어디에서도 커널 내에서 VS2012에서 중단 점을 추가하고 이전의 변수 정의와 STDDEV 라인을 포함 할 때 :

double mean, stddev, sumOfValues, sumOfValuesSquared; 
unsigned int n; 

// acquire greater than 0 values for: sumOfValues, sumOfValuesSquared, and n 

stddev = (float)(sqrt((double)(n) * sumOfValuesSquared - (sumOfValues*sumOfValues))/(double)(n)); 

을 중단 점에 도달하지 않으며 커널이 실행되지 않습니다. 그 한 줄을 제거하면 커널이 실행됩니다. sqrt와 관련이 있다고 생각했지만 그렇지 않습니다. 다른 줄이있다 :

mean = sumOfValues/n; 

나는 그 줄을 사용할 때도 커널을 실행하지 않는다. CUDA에서 타입 변환에 대해 빠뜨린 것은 무엇입니까 (레지스터 문제입니까, 단 정밀도와 배정 밀도입니까?).

- 나는 1 스레드의 수를 조정 한 다음 1024을 처음 실행, 그것은과 두 번째, 내 브레이크 포인트로 이동

- UPDATE (2013년 10월 2일 중부 표준시 14시 25분) 스레드 수가 많으면 커널이 실행되지 않습니다. 아래 코드를 참조하십시오.

#include "stdafx.h" 

#include <stdio.h> 
#include <cuda.h> 
#include <cuda_runtime.h> 
#include <device_launch_parameters.h> 

typedef struct 
{ 
    unsigned int value; 
} ValueStruct; 

__global__ void FailsToExecute(ValueStruct *vs) 
{ 
    unsigned int numerator = vs->value; 
    unsigned int denominator= 3; 
    bool eject = false; 

    if(denominator > 0) 
    { 
     if(1.0f * numerator/denominator > 17.98f) 
      eject = true; 
     else 
      eject = false; 
    } 
} 

int _tmain(int argc, _TCHAR* argv[]) 
{ 
    ValueStruct *vsHost; 
    ValueStruct *vsDevice; 

    cudaMallocHost((void **)&vsHost, sizeof(ValueStruct)); 
    cudaMalloc((void **)&vsDevice, sizeof(ValueStruct)); 

    vsHost->value = 54; 

    cudaMemcpy(vsDevice, vsHost, sizeof(ValueStruct), cudaMemcpyKind::cudaMemcpyHostToDevice); 

    dim3 blocks(5); 
    dim3 threads(1024); 

    FailsToExecute<<<blocks, threads>>>(vsDevice); 

    return 0; 
} 

레지스터 경계를 어떻게 계산합니까? 나는 그것에 대해 많이 모른다.

Answer 1

가용 자원 (예 : 레지스터, 공유 메모리)보다 많은 자원을 필요로하는 커널은 실행되지 않습니다.

https://devtalk.nvidia.com/default/topic/545591/how-to-debug-kernel-throwing-an-exception-/?offset=16

인해 각 GPU 아키텍쳐 특정 커널의 조합에 필요한 자원의 정확한 계산을 위해 다른 할당 단위의 효과 : 여기에서 도시 된 바와 같이 이것은 예를 들면, 적절한 오류 검사에 의해 검출 될 수있다 특정 발사 구성은 사소한 일이 될 수 있습니다. 이러한 이유로 세분화 된 세부 사항을 통합 한 CUDA 점유율 계산기를 사용할 것을 제안합니다.

http://developer.download.nvidia.com/compute/cuda/CUDA_Occupancy_calculator.xls

Answer 2

는 NVCC 컴파일러 멀리 아무것도 커널을 최적화하는 것이 가능 : 현재 점유 스프레드 시트를 찾을 수 있습니까? 커널 함수를 살펴보면, 실제로 아무 것도하지 않기 때문에 이것이 0 명령으로 안전하게 최적화 될 수있는 방법을 알 수있었습니다. eject 때문에 문제가되지 않는다 eject 설정

__global__ void FailsToExecute(ValueStruct *vs) 
{ 
    unsigned int numerator = vs->value; 
    unsigned int denominator= 3; 
    bool eject = false; 

    if(denominator > 0) 
    { 
     if(1.0f * numerator/denominator > 17.98f) 
      eject = true; 
     else 
      eject = false; 
    } 
} 

다시 사용되지 않습니다. 그래서 우리는 그 두 가지 과제를 배제 할 수 있습니다. if() 조건의 표현식은 아무 것도 수정하지 않으며 if 문 중 하나의 분기에 대해 아무 작업도 수행하지 않으므로 if()를 제거 할 수있는 것처럼 보입니다. 그리고 계속해서 커널의 맨 위로 돌아가서, 아무 것도 최적화하지 않고 커널이 똑같은 결과를 만들어내는 것처럼 보입니다.

bool 배열과 같은 출력을 추가하고 그 배열에 eject의 결과를 저장하면 커널이 실행되는 것을 볼 수 있습니다.