指针数组作为cuda kernel函数的参数

2016-01-19 05:43:44 646 阅读 AI 写同款 · GEO 优化AI 选题数据监测一键分发 ›

从Kernel Panic到CUDA Kernel：深入解析操作系统内核的设计哲学与工程实践内核（Kernel）是操作系统的核心组件，负责管理系统资源、提供硬件抽象层，并确保系统的安全与稳定运行。其核心原理在于通过划分用户空间与内核空间，利用CPU提供的不同特权级别（如Ring 0和Ring 3），实现对硬件和关键资源的受控访问。这种设计带来了显著的技术价值：它通过集中管理保障了系统安全，防止应用程序间的相互干扰；同时，通过减少不必要的上下文切换和权限检查，为需要直接硬件交互的任务（如GPU计算、网络包处理）提供了极致的性能基础。在应用场景上，无论是Linux的宏内核、VxWorks的微内核，还是阅读详情

我有一个程序，功能就是有一个3页的数据，高为Height，宽为Width，然后我一个block中的线程数为Height*Width，一维的，（这只是测试，用的Height和Width比较小，所以就这样分配吧），grid也是一维，大小是3，kernel函数的功能就是每个线程输出自己的blockIdx.x,threadIdx.x和所要处理的数据data。因为我在别的程序中必须要用到指针数组做函数新参数，所以这个程序只是对指针数组做函数参数做一个测试，没有什么实际的作用。可是一直不对，核函数不会有任何输出，所有线程好像都没有执行，实在不知道咋弄了，求各位帮帮忙！



#include<stdio.h>

#include<cuda_runtime.h>

#define Height 3

#define Width 5



__global__  void  printf_kernel(int **dev_ptr)

{

        if(blockIdx.x < 3)

        {

//printf("(%d,%d)\n",blockIdx.x,threadIdx.x);



        int pos=threadIdx.x;



        int *pptr=*(dev_ptr+blockIdx.x);



        int data=pptr[pos];



        printf("(%d,%d):  %d\n",blockIdx.x,threadIdx.x,data);



        }

}





int main()

{

        int a[3*Height*Width];

        int i,j,k;

        for(k=0;k<3;k++)

        {

                for(i=0;i<Height;i++)

                {

                        for(j=0;j<Width;j++)

                        {

                                a[k*Width*Height+i*Width+j]=k+i+j;

                                printf("%d  ",a[k*Height*Width+i*Width+j]);

                        }

                        printf("\n");

                }

                printf("\n");

                printf("\n");

        }



        int *dev_ptr[3];

        for(i=0;i<3;i++)

        {

                cudaMalloc((void**)&dev_ptr[i],sizeof(int)*Width*Height);



                cudaMemcpy(dev_ptr[i],a+i*Width*Height,sizeof(int)*Width*Height,cudaMemcpyHostToDevice);

        }





        dim3 block(Height*Width);

        dim3 grid(3);



        printf_kernel<<<grid,block>>>(dev_ptr);



        cudaDeviceSynchronize();



        return 0;

}