库达记忆障碍

我有一个CUDA内核,我正在编译成一个没有任何特殊标志的CUBIN文件:

nvcc text.cu -cubin

它编译了以下消息:

建议:假设全局内存空间,无法判断指针指向什么。

以及对某个临时cpp文件中一行的引用。我可以通过评论一些对我来说毫无意义的看似武断的代码来实现这一点。

内核如下:

__global__ void string_search(char** texts, int* lengths, char* symbol, int* matches, int symbolLength)
{
    int localMatches = 0;
    int blockId = blockIdx.x + blockIdx.y * gridDim.x;
    int threadId = threadIdx.x + threadIdx.y * blockDim.x;
    int blockThreads = blockDim.x * blockDim.y;

    __shared__ int localMatchCounts[32];

    bool breaking = false;
    for(int i = 0; i < (lengths[blockId] - (symbolLength - 1)); i += blockThreads)
    {
        if(texts[blockId][i] == symbol[0])
        {
            for(int j = 1; j < symbolLength; j++)
            {
                if(texts[blockId][i + j] != symbol[j])
                {
                    breaking = true;
                    break;
                }
            }
            if (breaking) continue;
            localMatches++;
        }
    }

    localMatchCounts[threadId] = localMatches;

    __syncthreads();

    if(threadId == 0)
    {
        int sum = 0;
        for(int i = 0; i < 32; i++)
        {
            sum += localMatchCounts[i];
        }
        matches[blockId] = sum;
    }
}

如果我换线

localMatchCounts[threadId] = localMatches;

在这条线的第一个for循环之后

localMatchCounts[threadId] = 5;

它编译时没有通知。这也可以通过注释行上方的循环中看似随机的部分来实现。我还尝试用普通数组替换本地内存数组,但没有效果。有人能告诉我是什么问题吗?

这个系统是vista 64位的,就其价值而言。

编辑:我修复了代码,这样它实际上可以工作,尽管它仍然会生成编译器的通知。似乎警告并不是一个问题,至少在正确性方面(它可能会影响性能)。