Surface memory surface memory does not work

siyam · June 16, 2011, 5:33pm

Hi this is my code. after calling the function “test” I print the array dtr1. 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[WH];
float dtr = new float[WH];
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;

}

siyam · June 16, 2011, 5:33pm

Hi this is my code. after calling the function “test” I print the array dtr1. 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[WH];
float dtr = new float[WH];
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;

}

brano · June 17, 2011, 7:24am

Hi this is my code. after calling the function “test” I print the array dtr1. 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;

}

Hi,

could it be that surf is of type void and when you access it with:

[font=arial, verdana, tahoma, sans-serif]surf2Dwrite(a, surfD, i,j, cudaBoundaryModeTrap);[/font]

[font=“arial, verdana, tahoma, sans-serif”]you should in fact be using:[/font]

[font=“arial, verdana, tahoma, sans-serif”]surf2Dwrite(a, surfD, 4*i,j, cudaBoundaryModeTrap);[/font]

[font=“arial, verdana, tahoma, sans-serif”]

[/font]

[font=“arial, verdana, tahoma, sans-serif”]Also you need to specify allocation of 2D array:[/font]

[font=“arial, verdana, tahoma, sans-serif”]cudaMallocArray(&cuArrD, &channelDesc, W, H, cudaArraySurfaceLoadStore);[/font]

brano · June 17, 2011, 7:24am

Hi this is my code. after calling the function “test” I print the array dtr1. 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;

}

Hi,

could it be that surf is of type void and when you access it with:

[font=arial, verdana, tahoma, sans-serif]surf2Dwrite(a, surfD, i,j, cudaBoundaryModeTrap);[/font]

[font=“arial, verdana, tahoma, sans-serif”]you should in fact be using:[/font]

[font=“arial, verdana, tahoma, sans-serif”]surf2Dwrite(a, surfD, 4*i,j, cudaBoundaryModeTrap);[/font]

[font=“arial, verdana, tahoma, sans-serif”]

[/font]

[font=“arial, verdana, tahoma, sans-serif”]Also you need to specify allocation of 2D array:[/font]

[font=“arial, verdana, tahoma, sans-serif”]cudaMallocArray(&cuArrD, &channelDesc, W, H, cudaArraySurfaceLoadStore);[/font]

siyam · June 17, 2011, 8:43am

Hi Thank you for your reply. But it doesnt work…

siyam · June 17, 2011, 8:43am

Hi Thank you for your reply. But it doesnt work…

siyam · June 17, 2011, 9:28am

Hi,

It works… the changes should be…

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

to

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

and the changes suggested by Brano…

siyam · June 17, 2011, 9:28am

Hi,

It works… the changes should be…

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

to

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

and the changes suggested by Brano…

brano · June 17, 2011, 2:35pm

Hi,

just a small notice:

&dtr1[0] = dtr1

It is the same thing. :)

brano · June 17, 2011, 2:35pm

Hi,

just a small notice:

&dtr1[0] = dtr1

It is the same thing. :)

Topic		Replies	Views
[Beginner] Memory is reseted in the kernel CUDA Programming and Performance	5	1318	October 29, 2010
Odd behavior when reading from texture Texture and Surface memory am I missing something CUDA Programming and Performance	9	13072	April 23, 2011
Corruption in memory copy? CUDA Programming and Performance	3	4010	October 15, 2010
3D surface memory bug? CUDA Programming and Performance	1	1185	May 21, 2015
Inconsistent Cuda Errors CUDA Programming and Performance	10	1059	July 7, 2017
Using texture memory over iterations causes incorrect read/write of some lines CUDA Programming and Performance cuda	2	513	September 2, 2020
Layered 2D surface object reading problem CUDA Programming and Performance	7	1295	September 8, 2022
Undefined tex1Dfetch in kernel CUDA Programming and Performance	7	2789	March 11, 2021
2d array testing in very simple code using CUDA CUDA Programming and Performance	29	30403	November 15, 2010
Using Textures CUDA Programming and Performance	10	21810	March 29, 2007

Surface memory surface memory does not work

Related topics