An Introduction to OpenCL Programming

CaspianSea

于 2015-05-20 07:17:04 发布

阅读量898

点赞数

分类专栏： Graphics 文章标签： OpenCL

Graphics 专栏收录该内容

15 篇文章 0 订阅

订阅专栏

Benedict R. Gaster (AMD Architect) has published on AMD developers website, an introduction to OpenCL programming.

I repoduced the complete source code here without the comment (you have to jump to AMD’s website to read them!). I also removed all checkErr() to make the code smaller. The goal of this OpenCL program is to execute a kernel that copy the string “hello” from one buffer to another one. That’s all!

You can download OpenCL headers HERE.
The tutorial uses the C++ bindings header (cl.hpp) you can get HERE.
The OpenCL forum for developers can be found HERE.

But to successfully compile an OpenCL program, yuo must have the OpenCL.lib that is shipped with an OpenCL-ready graphics driver… NVIDIA has such a driver but it’s currently reserved to registered developers.

 
 #define __NO_STD_VECTOR	
#define __NO_STD_STRING 
#include <CL/cl.hpp>
 
#include <cstdio>
#include <cstdlib>
#include <fstream>
#include <iostream>
#include <string>
#include <iterator>
 
const std::string hw("Hello World\n");
 
inline void
checkErr(cl_int err, const char * name)
{
 if (err != CL_SUCCESS) 
 {
   std::cerr << "ERROR: " << name
      << " (" << err << ")" << std::endl;
   exit(EXIT_FAILURE);
 }
}
 
int main(void)
{
  cl_int err;
  cl::Context context(
    CL_DEVICE_TYPE_CPU, 
    NULL,
    NULL,
    NULL,
    &err);
 
  char * outH = new char[hw.length()+1];
  cl::Buffer outCL(
    context,
    CL_MEM_WRITE_ONLY | CL_MEM_USE_HOST_PTR,
    hw.length()+1,
    outH,
    &err);
  
  cl::vector<cl::Device> devices;
  devices = context.getInfo<CL_CONTEXT_DEVICES>();
  
  std::ifstream file("lesson1_kernels.cl");
 
  std::string prog(
    std::istreambuf_iterator<char>(file),
    (std::istreambuf_iterator<char>()));
 
  cl::Program::Sources source(
    1,
    std::make_pair(prog.c_str(), prog.length()+1));
 
  cl::Program program(context, source);
  err = program.build(devices,"");
  
  cl::Kernel kernel(program, "hello", &err);
 
  err = kernel.setArg(0, outCL);
  
  cl::CommandQueue queue(context, devices[0], 0, &err);
 
  cl::Event event;
  err = queue.enqueueNDRangeKernel(
    kernel, 
    cl::NullRange,
    cl::NDRange(hw.length()+1),
    cl::NDRange(1, 1), 
    NULL, 
    &event);
  
  event.wait();    
  err = queue.enqueueReadBuffer(
    outCL,
    CL_TRUE,
    0,
    hw.length()+1,
    outH);
  std::cout << outH;
  return EXIT_SUCCESS;
}  
 
__constant char hw[] = "Hello World\n";
__kernel void hello(__global char * out)
{
    size_t tid = get_global_id(0);
    out[tid] = hw[tid];
}