CUDA Array/Surface Memory

Question

After calling the function test, I print the dtr1 array. I am expecting to get 100 for all the elements, but I am not getting it. why is that?

#include "ImageUtil2D.h"
#define W 10
#define H 10
#define MAX 100000
#define No_THREADS 10
surface<void,2> surfD;

__global__ void test()
{
for(int i=0;i<W;i++)
    for(int j=0;j<H;j++)
    {
        float a=100;
        surf2Dwrite(a, surfD, i,j, cudaBoundaryModeTrap);
    }
}

int main()
{
int *image = new int[W*H];
float *dtr = new float[W*H];
ImageUtil2D::InitImg(image, dtr, W, H);
const size_t sizef = size_t(W*H)*sizeof(float);

cudaChannelFormatDesc channelDesc = cudaCreateChannelDesc(32, 0, 0, 0, cudaChannelFormatKindFloat);
cudaArray* cuArrD;
cudaMallocArray(&cuArrD, &channelDesc, W*H, 0, cudaArraySurfaceLoadStore);
//cudaMemcpyToArray(cuArrD, 0, 0, dtr, sizef, cudaMemcpyHostToDevice);
cudaBindSurfaceToArray(surfD, cuArrD);

test<<<1, 1>>>();

float *dtr1=new float[W*H];
cudaMemcpyFromArray(&dtr1, cuArrD, 0, 0, sizef, cudaMemcpyDeviceToHost );
ImageUtil2D::Print(dtr1);
return 0;
}

Add the error handling code around the cuda api calls and post where and how it fails. — fabmilo
– fabmilo, Commented Jun 16, 2011 at 20:03

pQB · Accepted Answer · 2011-06-17 07:13:35Z

5

CUDA C Programming Guide 3.2. Section: 3.2.4.2.2 Surface Binding

Unlike texture memory, surface memory uses byte addressing. This means that the x-coordinate used to access a texture element via texture functions needs to be multiplied by the byte size of the element to access the same element via a surface function.

Try this:

surf2Dwrite(a, surfD, i * 4, j, cudaBoundaryModeTrap);

Hope this help.

Suggestion: Read the whole chapter about Surface Memory or you will get Read/Write Coherency problems before you excepted ;)

answered Jun 17, 2011 at 7:13

pQB

3,1374 gold badges25 silver badges51 bronze badges

Sign up to request clarification or add additional context in comments.

1 Comment

pQB Over a year ago

Oh, my apologies, i was almost sure. I've made a quick test and there is an extrange issue with cudaMemcpyFromArray(&dtr1, cuArrD, 0, 0, sizef, cudaMemcpyDeviceToHost );

Vitality · Accepted Answer · 2015-09-01 09:43:22Z

1

The additional issue pointed out by pQB in the comment to his own answer on

cudaMemcpyFromArray(&dtr1, cuArrD, 0, 0, sizef, cudaMemcpyDeviceToHost );

can be fixed by changing the above line to

cudaMemcpyFromArray(dtr1, cuArrD, 0, 0, sizef, cudaMemcpyDeviceToHost );

edited Sep 1, 2015 at 9:43

answered Sep 1, 2015 at 8:04

Vitality

21.7k5 gold badges118 silver badges153 bronze badges

Collectives™ on Stack Overflow

CUDA Array/Surface Memory

2 Answers 2

1 Comment

Comments

Your Answer

Hot Network Questions

Collectives™ on Stack Overflow

2 Answers 2

1 Comment

Comments

Your Answer

Sign up or log in

Post as a guest

Related