/*============================================================================Name        : OpenCLTest.cAuthor      : Zenny ChenVersion     :Copyright   : Your copyright noticeDescription : Hello World in C, Ansi-style============================================================================*/#include <stdio.h>
#include <string.h>
#include <stdlib.h>
#include <unistd.h>
#include <CL/cl.h>static int GetCurrentLocationFilePath(char pDst[512], const char *filename)
{if(pDst == NULL || filename == NULL)return 0;int size = readlink("/proc/self/exe", pDst, 512);while(pDst[size - 1] != '/')size--;strcpy(&pDst[size], filename);int retSize = strlen(filename) + size;pDst[retSize] = '\0';return retSize;
}int main(void)
{/*Step1: Getting platforms and choose an available one.*/cl_uint numPlatforms;   //the NO. of platformscl_int  status = clGetPlatformIDs(0, NULL, &numPlatforms);if (status != CL_SUCCESS){puts("Error: Getting platforms!");return 0;}cl_platform_id platforms[16];/*For clarity, choose the first available platform. */if(numPlatforms > 0){status = clGetPlatformIDs(numPlatforms, platforms, NULL);if(status != CL_SUCCESS){puts("Failed to get platform IDs");return 0;}}/*Step 2:Query the platform and choose the first GPU device if has one.Otherwise use the CPU as device.*/cl_uint             numDevices = 0;cl_device_id        devices[16];clGetDeviceIDs(platforms[0], CL_DEVICE_TYPE_GPU, 0, NULL, &numDevices);if(numDevices == 0)    //no GPU available.
    {puts("No devices available!");return 0;}else{printf("The number of available devices is: %u\n", numDevices);clGetDeviceIDs(platforms[0], CL_DEVICE_TYPE_GPU, numDevices, devices, NULL);}/*Step 3: Create context.*/cl_context context = clCreateContext(NULL,1, devices,NULL,NULL,NULL);/*Step 4: Creating command queue associate with the context.*/cl_command_queue commandQueue = clCreateCommandQueue(context, devices[0], 0, NULL);/*Step 5: Create program object */char filePath[512];GetCurrentLocationFilePath(filePath, "test.cl");FILE *fp = fopen(filePath, "r");if(fp == NULL){puts("OpenCL kernel source file open failed!");return 0;}fseek(fp, 0, SEEK_END);long fileLength = ftell(fp);fseek(fp, 0, SEEK_SET);char *source = (char*)malloc(fileLength + 1);fread(source, 1, fileLength, fp);fclose(fp);size_t sourceSize[] = {fileLength};cl_program program = clCreateProgramWithSource(context, 1, (const char**)&source, sourceSize, NULL);free(source);if(program == NULL){puts("Failed to create the program!");return 0;}/*Step 6: Build program. */status = clBuildProgram(program, 1,devices,NULL,NULL,NULL);if(status != CL_SUCCESS){puts("Failed to build the program!");return 0;}/*Step 7: Initial input,output for the host and create memory objects for the kernel*/int input[128];for(int i = 0; i < 128; i++)input[i] = i + 1;cl_mem inputBuffer = clCreateBuffer(context, CL_MEM_READ_ONLY|CL_MEM_COPY_HOST_PTR, sizeof(input), input, NULL);cl_mem outputBuffer = clCreateBuffer(context, CL_MEM_WRITE_ONLY , sizeof(input), NULL, NULL);/*Step 8: Create kernel object */cl_kernel kernel = clCreateKernel(program, "test", NULL);/*Step 9: Sets Kernel arguments.*/status = clSetKernelArg(kernel, 0, sizeof(cl_mem), &inputBuffer);status = clSetKernelArg(kernel, 1, sizeof(cl_mem), &outputBuffer);/*Step 10: Running the kernel.*/size_t global_work_size[1] = { 128 };status = clEnqueueNDRangeKernel(commandQueue, kernel, 1, NULL, global_work_size, NULL, 0, NULL, NULL);/*Step 11: Read the cout put back to host memory.*/int output[128];status = clEnqueueReadBuffer(commandQueue, outputBuffer, CL_TRUE, 0, sizeof(input), output, 0, NULL, NULL);/*Step 12: Clean the resources.*/status = clReleaseKernel(kernel);               //Release kernel.status = clReleaseProgram(program);             //Release the program object.status = clReleaseMemObject(inputBuffer);       //Release mem object.status = clReleaseMemObject(outputBuffer);status = clReleaseCommandQueue(commandQueue);   //Release  Command queue.status = clReleaseContext(context);             //Release context.for(int i = 0; i < 128; i++){if(output[i] != i + 2){printf("Error occurred @%d!", i);return 0;}}puts("Pass!");return 1;
}

/*============================================================================Name        : OpenCLTest.cAuthor      : Zenny ChenVersion     :Copyright   : Your copyright noticeDescription : Simple OpenCL kernel source============================================================================*/__kernel void test(__global int* in, __global int* out)
{int index = get_global_id(0);out[index] = in[index] + 1;
}