//------------------------------------------------------------------------------
int main(int, char**) {
print_platforms();
return 0;
}
int main(int argc, char **argv) {
cl_int status;
const char *platform_name = "NVIDIA";
if (!find_platform(platform_name, &platform)) {
fprintf(stderr,"Error: Platform \"%s\" not found\n", platform_name);
print_platforms();
teardown(-1);
}
status = clGetDeviceIDs(platform, CL_DEVICE_TYPE_ALL, 1, &device, NULL);
checkError (status, "Error: could not query devices");
context = clCreateContext(NULL, 1, &device, NULL, NULL, &status);
checkError(status, "could not create context");
const char name[] = KERNELDIR "/reduce.cl";
unsigned char *source;
size_t size;
if (!load_file(name, &source, &size)) {
teardown(-1);
}
program = clCreateProgramWithSource(context, 1, (const char **) &source, &size, &status);
checkError(status, "Error: failed to create program %s: ", name);
status = clBuildProgram(program, 1, &device, "-I.", NULL, NULL);
if (status != CL_SUCCESS) {
print_build_log(program, device);
checkError(status, "Error: failed to create build %s: ", name);
}
free(source);
print_device_info(device, 0);
queue = clCreateCommandQueue(context, device, CL_QUEUE_PROFILING_ENABLE, &status);
checkError(status, "could not create command queue");
cl_ulong start, end;
cl_event event;
size_t width = 1024+1024;
size_t buf_size = width*sizeof(cl_float);
kernel = clCreateKernel(program, "reduce", &status);
checkError(status, "could not create kernel");
size_t work_size = width;
size_t local_size = 64;
size_t local_buf_size = local_size * sizeof(cl_float);
size_t groups = width / local_size;
size_t res_buf_size = groups * sizeof(cl_float);
float *data_in = malloc(buf_size);
float *data_out = malloc(res_buf_size);
if (!data_in || !data_out) {
fprintf(stderr,"\nError: malloc failed\n");
teardown(-1);
}
for (unsigned int i = 0; i < width; ++i) {
data_in[i] = (float) (i % 16);
}
buffer_in = clCreateBuffer(context, CL_MEM_READ_WRITE, buf_size, NULL, &status);
checkError(status, "Error: could not create buffer_in");
buffer_out = clCreateBuffer(context, CL_MEM_READ_WRITE, res_buf_size, NULL, &status);
checkError(status, "Error: could not create buffer_out");
status = clEnqueueWriteBuffer(queue, buffer_in, CL_FALSE, 0, buf_size, data_in, 0, NULL, NULL);
checkError(status, "Error: could not copy data into device");
// execute kernel
int arg = 0;
status = clSetKernelArg(kernel, arg++, sizeof(cl_mem), &buffer_in);
status = clSetKernelArg(kernel, arg++, sizeof(cl_mem), &buffer_out);
status = clSetKernelArg(kernel, arg++, local_buf_size, NULL);
status = clSetKernelArg(kernel, arg++, sizeof(cl_int), &width);
checkError(status, "Error: could not set args");
status = clEnqueueNDRangeKernel(queue, kernel, 1, NULL, &work_size, &local_size, 0, NULL, &event);
checkError(status, "Error: could not enqueue kernel");
status = clWaitForEvents(1, &event);
checkError(status, "Error: could not wait for event");
status = clGetEventProfilingInfo(event, CL_PROFILING_COMMAND_START, sizeof(cl_ulong), &start, NULL);
checkError(status, "Error: could not get start profile information");
status = clGetEventProfilingInfo(event, CL_PROFILING_COMMAND_END, sizeof(cl_ulong), &end, NULL);
checkError(status, "Error: could not get end profile information");
status = clReleaseEvent(event);
checkError(status, "Error: could not release event");
// read results back
status = clEnqueueReadBuffer(queue, buffer_out, CL_TRUE, 0, res_buf_size, data_out, 0, NULL, NULL);
checkError(status, "Error: could not copy data into device");
status = clFinish(queue);
checkError(status, "Error: could not finish successfully");
float clsum = 0;
for (unsigned int i = 0; i < groups; ++i) {
clsum += data_out[i];
}
#ifdef DEBUG
for (int i = 0; i < groups; ++i) {
printf("%.0f ", data_out[i]);
}
#endif
double elapsed = (end - start) * 1e-9f;
printf("time: %f\n", elapsed);
float sum = 0;
for (unsigned int i = 0; i < width; ++i) {
sum += data_in[i];
}
if (sum != clsum)
fprintf(stderr, "Compare failed: %f != %f\n", clsum, sum);
free(data_in);
free(data_out);
teardown(0);
}
int main(int argc, char **argv) {
cl_int status;
const char *platform_name = "NVIDIA";
if (!find_platform(platform_name, &platform)) {
fprintf(stderr,"Error: Platform \"%s\" not found\n", platform_name);
print_platforms();
teardown(-1);
}
status = clGetDeviceIDs(platform, CL_DEVICE_TYPE_ALL, 1, &device, NULL);
checkError (status, "Error: could not query devices");
context = clCreateContext(NULL, 1, &device, NULL, NULL, &status);
checkError(status, "could not create context");
const char name[] = KERNELDIR "/gauss.cl";
unsigned char *source;
size_t size;
if (!load_file(name, &source, &size)) {
teardown(-1);
}
program = clCreateProgramWithSource(context, 1, (const char **) &source, &size, &status);
checkError(status, "Error: failed to create program %s: ", name);
status = clBuildProgram(program, 1, &device, "-I.", NULL, NULL);
if (status != CL_SUCCESS) {
print_build_log(program, device);
checkError(status, "Error: failed to create build %s: ", name);
}
free(source);
print_device_info(device, 0);
queue = clCreateCommandQueue(context, device, CL_QUEUE_PROFILING_ENABLE, &status);
checkError(status, "could not create command queue");
cl_ulong start, end;
cl_event event;
unsigned char *data;
size_t datasize;
if (!load_file("lena.dat", &data, &datasize)) {
teardown(-1);
}
size_t width = 512;
size_t height = 512;
size_t buf_size = width*height*sizeof(cl_float);
float *data_out = malloc(buf_size);
if (!data_out) {
fprintf(stderr,"\nError: malloc failed\n");
teardown(-1);
}
kernel = clCreateKernel(program, "gauss", &status);
checkError(status, "could not create kernel");
cl_image_format format = { CL_R, CL_UNORM_INT8};
buffer_in = clCreateImage2D (context, CL_MEM_READ_ONLY | CL_MEM_COPY_HOST_PTR, &format,
width, height, 0,
data,
&status);
checkError(status, "Error: could not create image");
buffer_out = clCreateBuffer(context, CL_MEM_READ_WRITE, buf_size, NULL, &status);
checkError(status, "Error: could not create buffer_out");
// execute kernel
int arg = 0;
status = clSetKernelArg(kernel, arg++, sizeof(cl_mem), &buffer_in);
status = clSetKernelArg(kernel, arg++, sizeof(cl_mem), &buffer_out);
checkError(status, "Error: could not set args");
size_t work_size[] = {width, height};
size_t local_size[] = {1, 1};
status = clEnqueueNDRangeKernel(queue, kernel, 2, NULL, work_size, local_size, 0, NULL, &event);
checkError(status, "Error: could not enqueue kernel");
status = clWaitForEvents(1, &event);
checkError(status, "Error: could not wait for event");
status = clGetEventProfilingInfo(event, CL_PROFILING_COMMAND_START, sizeof(cl_ulong), &start, NULL);
checkError(status, "Error: could not get start profile information");
status = clGetEventProfilingInfo(event, CL_PROFILING_COMMAND_END, sizeof(cl_ulong), &end, NULL);
checkError(status, "Error: could not get end profile information");
status = clReleaseEvent(event);
checkError(status, "Error: could not release event");
// read results back
status = clEnqueueReadBuffer(queue, buffer_out, CL_FALSE, 0, buf_size, data_out, 0, NULL, NULL);
checkError(status, "Error: could not copy data into device");
status = clFinish(queue);
checkError(status, "Error: could not finish successfully");
double elapsed = (end - start) * 1e-9f;
printf("time: %f\n", elapsed);
write_bmp("gauss.bmp", data_out, width, height, NORMAL);
free(data);
free(data_out);
teardown(0);
}
