使用FFI从Haskell调用CUDA"Hello World"会产生错误的结果

Question

这是标准的Hello World CUDA文件:

#include <stdio.h>
#include "hello.h"

const int N = 7;
const int blocksize = 7;

__global__ void hello_kernel(char *a, int *b) {
    a[threadIdx.x] += b[threadIdx.x];
}

#define cudaCheckError() { \
    cudaError_t e=cudaGetLastError(); \
    if(e!=cudaSuccess) { \
        printf("Cuda failure %s:%d: '%s'\n",__FILE__,__LINE__,cudaGetErrorString(e)); \
        exit(0); \
    } \
}

void hello() {
    char a[N] = "Hello ";
    int b[N] = {15, 10, 6, 0, -11, 1, 0};

    char *ad;
    int *bd;
    const int csize = N*sizeof(char);
    const int isize = N*sizeof(int);

    printf("%s", a);

    cudaMalloc( (void**)&ad, csize );
    cudaMemcpy( ad, a, csize, cudaMemcpyHostToDevice );
    cudaCheckError();

    cudaMalloc( (void**)&bd, isize );
    cudaMemcpy( bd, b, isize, cudaMemcpyHostToDevice );
    cudaCheckError();

    dim3 dimBlock( blocksize, 1 );
    dim3 dimGrid( 1, 1 );
    hello_kernel<<<dimGrid, dimBlock>>>(ad, bd);
    cudaMemcpy( a, ad, csize, cudaMemcpyDeviceToHost );
    cudaCheckError();

    cudaFree( ad );
    cudaCheckError();

    printf("%s\n", a);
}

它的标题:

-- hello.h
extern "C" 
void hello();

这是一个调用这个函数的Haskell文件:

-- test.hs
{-# LANGUAGE ForeignFunctionInterface #-}

import Foreign.C
import Foreign.Ptr (Ptr,nullPtr)

foreign import ccall "hello" hello :: IO ()

main = hello

我正在编译它:

nvcc hello.c -c -o hello.o
ghc test.hs -o test hello.o -L/usr/local/cuda/lib -optl-lcudart

运行该程序的./test结果如下:

Hello Cuda failure hello.cu:32: 'no CUDA-capable device is detected'

运行与C相同的程序main(),只是要求hello生产Hello World,符合市场预期.

如何让Haskell正确检测设备？

Answer 1

也许不相关,但我能够在Mac上使用单独的板载和独立显卡重现您的错误.当在"系统偏好设置"中启用"自动图形切换"(并且没有运行3D图形应用程序)时,我得到相同的"没有检测到支持CUDA的设备"错误.

当我关闭自动图形切换时,它会强制Mac使用独立显卡,然后程序按预期运行.

纯粹基于C/CUDA的代码版本似乎不受此首选项的影响,并且无论是否启用自动切换,它始终有效.