fork download
copy 
  1. /**********************************************************************
  2. Copyright ©2014 Advanced Micro Devices, Inc. All rights reserved.
  3.  
  4. Redistribution and use in source and binary forms, with or without modification, are permitted provided that the following conditions are met:
  5.  
  6. 	Redistributions of source code must retain the above copyright notice, this list of conditions and the following disclaimer.
  7. 	Redistributions in binary form must reproduce the above copyright notice, this list of conditions and the following disclaimer in the documentation and/or
  8.  other materials provided with the distribution.
  9.  
  10. THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS "AS IS" AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT LIMITED TO, THE IMPLIED
  11.  WARRANTIES OF MERCHANTABILITY AND FITNESS FOR A PARTICULAR PURPOSE ARE DISCLAIMED. IN NO EVENT SHALL THE COPYRIGHT HOLDER OR CONTRIBUTORS BE LIABLE FOR ANY
  12.  DIRECT, INDIRECT, INCIDENTAL, SPECIAL, EXEMPLARY, OR CONSEQUENTIAL DAMAGES (INCLUDING, BUT NOT LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS
  13.  OF USE, DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT (INCLUDING
  14.  NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
  15. ********************************************************************/
  16.  
  17. // For clarity,error checking has been omitted.
  18.  
  19. #include <CL/cl.h>
  20. #include <string.h>
  21. #include <stdio.h>
  22. #include <stdlib.h>
  23. #include <iostream>
  24. #include <string>
  25. #include <fstream>
  26.  
  27. #define SUCCESS 0
  28. #define FAILURE 1
  29.  
  30. using namespace std;
  31.  
  32. /* convert the kernel file into a string */
  33. int convertToString(const char *filename, std::string& s)
  34. {
  35. 	size_t size;
  36. 	char*  str;
  37. 	std::fstream f(filename, (std::fstream::in | std::fstream::binary));
  38.  
  39. 	if(f.is_open())
  40. 	{
  41. 		size_t fileSize;
  42. 		f.seekg(0, std::fstream::end);
  43. 		size = fileSize = (size_t)f.tellg();
  44. 		f.seekg(0, std::fstream::beg);
  45. 		str = new char[size+1];
  46. 		if(!str)
  47. 		{
  48. 			f.close();
  49. 			return 0;
  50. 		}
  51.  
  52. 		f.read(str, fileSize);
  53. 		f.close();
  54. 		str[size] = '\0';
  55. 		s = str;
  56. 		delete[] str;
  57. 		return 0;
  58. 	}
  59. 	cout<<"Error: failed to open file\n:"<<filename<<endl;
  60. 	return FAILURE;
  61. }
  62.  
  63. int main(int argc, char* argv[])
  64. {
  65.  
  66. 	/*Step1: Getting platforms and choose an available one.*/
  67. 	cl_uint numPlatforms;	//the NO. of platforms
  68. 	cl_platform_id platform = NULL;	//the chosen platform
  69. 	cl_int	status = clGetPlatformIDs(0, NULL, &numPlatforms);
  70. 	if (status != CL_SUCCESS)
  71. 	{
  72. 		cout << "Error: Getting platforms!" << endl;
  73. 		return FAILURE;
  74. 	}
  75.  
  76. 	/*For clarity, choose the first available platform. */
  77. 	if(numPlatforms > 0)
  78. 	{
  79. 		cl_platform_id* platforms = (cl_platform_id* )malloc(numPlatforms* sizeof(cl_platform_id));
  80. 		status = clGetPlatformIDs(numPlatforms, platforms, NULL);
  81. 		platform = platforms[0];
  82. 		free(platforms);
  83. 	}
  84.  
  85. 	/*Step 2:Query the platform and choose the first GPU device if has one.Otherwise use the CPU as device.*/
  86. 	cl_uint				numDevices = 0;
  87. 	cl_device_id        *devices;
  88. 	status = clGetDeviceIDs(platform, CL_DEVICE_TYPE_GPU, 0, NULL, &numDevices);	
  89. 	if (numDevices == 0)	//no GPU available.
  90. 	{
  91. 		cout << "No GPU device available." << endl;
  92. 		cout << "Choose CPU as default device." << endl;
  93. 		status = clGetDeviceIDs(platform, CL_DEVICE_TYPE_CPU, 0, NULL, &numDevices);	
  94. 		devices = (cl_device_id*)malloc(numDevices * sizeof(cl_device_id));
  95. 		status = clGetDeviceIDs(platform, CL_DEVICE_TYPE_CPU, numDevices, devices, NULL);
  96. 	}
  97. 	else
  98. 	{
  99. 		devices = (cl_device_id*)malloc(numDevices * sizeof(cl_device_id));
  100. 		status = clGetDeviceIDs(platform, CL_DEVICE_TYPE_GPU, numDevices, devices, NULL);
  101. 	}
  102.  
  103.  
  104. 	/*Step 3: Create context.*/
  105. 	cl_context context = clCreateContext(NULL,1, devices,NULL,NULL,NULL);
  106.  
  107. 	/*Step 4: Creating command queue associate with the context.*/
  108. 	/*old func. code
  109. 		cl_command_queue commandQueue = clCreateCommandQueue(context, devices[0], 0, NULL);
  110.     	*/
  111. 	/*new func.
  112.     	*	cl_command_queue clCreateCommandQueueWithProperties(
  113. 			cl_context context, 
  114. 			cl_device_id device, 
  115. 			const cl_queue_properties *properties, 
  116. 			cl_int *errcode_ret)
  117. 	*/
  118. 	cl_command_queue commandQueue = clCreateCommandQueueWithProperties(context, devices[0], 0, NULL);
  119. 	//cl_command_queue commandQueue = clCreateCommandQueue(context, devices[0], 0, NULL);
  120.  
  121. 	/*Step 5: Create program object */
  122. 	const char *filename = "HelloWorld_Kernel.cl";
  123. 	string sourceStr;
  124. 	status = convertToString(filename, sourceStr);
  125. 	const char *source = sourceStr.c_str();
  126. 	size_t sourceSize[] = {strlen(source)};
  127. 	cl_program program = clCreateProgramWithSource(context, 1, &source, sourceSize, NULL);
  128.  
  129. 	/*Step 6: Build program. */
  130. 	const char options[] = "-cl-std=CL2.0";
  131. 	status = clBuildProgram(program, 1,devices, options,NULL,NULL);
  132.  
  133. 	/*Step 7: Create kernel object */
  134. 	cl_kernel kernel = clCreateKernel(program,"SVMhelloworld", NULL);
  135.  
  136. 	/*Step 8: Initial input,output for the host and create SVM buffer*/
  137. 	const char *input = "HelloWorld";
  138. 	size_t strlength = strlen(input);
  139. 	char *output = (char*) malloc(strlength + 1);
  140. 	void *inputBuffer = clSVMAlloc( context, CL_MEM_READ_WRITE, (strlength + 1) * sizeof(char), 0 );
  141. 	void *outputBuffer = clSVMAlloc( context, CL_MEM_READ_WRITE, (strlength + 1) * sizeof(char), 0 );
  142.  
  143. 	status = clEnqueueSVMMap(commandQueue, CL_TRUE, CL_MAP_WRITE_INVALIDATE_REGION, inputBuffer, (strlength + 1) * sizeof(char), 0, NULL, NULL);
  144. 	memcpy(inputBuffer,input,strlength);
  145. 	cout << "input string:" << endl;
  146. 	cout << input << endl;
  147. 	/*test inputBuffer
  148. 	cout << "inputBuffer first char:" << endl;
  149. 	cout << *((char *)inputBuffer) << endl;
  150. 	*/
  151. 	status = clEnqueueSVMUnmap(commandQueue, inputBuffer, 0, NULL, NULL);
  152.  
  153. 	/*Step 9: Sets Kernel arguments.*/
  154. 	status = clSetKernelArgSVMPointer(kernel,0,(void *)(inputBuffer));
  155.     	status = clSetKernelArgSVMPointer(kernel,1,(void *)(outputBuffer));
  156.  
  157. 	/*Step 10: Running the kernel.*/
  158. 	size_t global_work_size[1] = {strlength};
  159. 	status = clEnqueueNDRangeKernel(commandQueue, kernel, 1, NULL, global_work_size, NULL, 0, NULL, NULL);
  160.  
  161.   	status = clEnqueueSVMMap(commandQueue, CL_TRUE, CL_MAP_WRITE_INVALIDATE_REGION, outputBuffer, (strlength + 1) * sizeof(char), 0, NULL, NULL);
  162. 	memcpy(output,outputBuffer,strlength);
  163. 	output[strlength] = '\0';	//Add the terminal character to the end of output.
  164.  
  165. 	/*test if kernel works and char. are all assign to outputBuffer*/
  166. 	int i;
  167. 	for(i = 0; i < 10; i++){
  168. 		cout <<"#" << i << ":" << *(((char *)outputBuffer)+i) << endl;
  169. 	}
  170.  
  171. 	cout << "\noutput string:" << endl;
  172. 	cout << output << endl;
  173.  
  174.   	status = clEnqueueSVMUnmap(commandQueue, outputBuffer, 0, NULL, NULL);
  175.  
  176. 	/*Step 12: Clean the resources.*/
  177. 	clSVMFree(context, inputBuffer);  
  178.     	clSVMFree(context, outputBuffer);  
  179. 	status = clReleaseKernel(kernel);				//Release kernel.
  180. 	status = clReleaseProgram(program);				//Release the program object.
  181. 	status = clReleaseCommandQueue(commandQueue);	//Release  Command queue.
  182. 	status = clReleaseContext(context);				//Release context.
  183.  
  184. 	if (output != NULL)
  185. 	{
  186. 		free(output);
  187. 		output = NULL;
  188. 	}
  189.  
  190. 	if (devices != NULL)
  191. 	{
  192. 		free(devices);
  193. 		devices = NULL;
  194. 	}
  195.  
  196. 	cout<<"Program passed!\n";
  197. 	return SUCCESS;
  198. }
Compilation error #stdin compilation error #stdout 0s 0KB
comments (?)
stdin
copy 
Standard input is empty
compilation info 
prog.c:19:19: fatal error: CL/cl.h: No such file or directory
compilation terminated.
stdout
copy 
Standard output is empty
https://ideone.com/KGhkWn
language:
C (gcc 8.3)
created:
10 years ago
visibility:
public

Share or Embed source code

Discover > Sphere Engine API

The brand new service which powers Ideone!

Discover > IDE Widget

Widget for compiling and running the source code in a web browser!