{"id":2538,"date":"2013-05-19T16:19:57","date_gmt":"2013-05-19T07:19:57","guid":{"rendered":"http:\/\/peta.okechan.net\/blog\/?p=2538"},"modified":"2013-05-20T00:13:24","modified_gmt":"2013-05-19T15:13:24","slug":"%e3%81%84%e3%81%bexcode%e3%81%a7opencl%e3%82%92%e3%81%af%e3%81%98%e3%82%81%e3%82%8b%e5%a4%9a%e5%88%86%e3%81%84%e3%81%a1%e3%81%b0%e3%82%93%e7%b0%a1%e5%8d%98%e3%81%8b%e3%82%82%e3%81%97%e3%82%8c%e3%81%aa","status":"publish","type":"post","link":"https:\/\/peta.okechan.net\/blog\/archives\/2538","title":{"rendered":"\u3044\u307eXcode\u3067OpenCL\u3092\u306f\u3058\u3081\u308b\u591a\u5206\u3044\u3061\u3070\u3093\u7c21\u5358\u304b\u3082\u3057\u308c\u306a\u3044\u65b9\u6cd5"},"content":{"rendered":"

\u4ee5\u524d\u66f8\u3044\u305fCUDA\u306e\u8a18\u4e8b<\/a>\u306eOpenCL\u7248\u3002
\n\u3053\u3061\u3089\u3082\u3001\u3044\u3061\u3070\u3093\u7c21\u5358\u306a\u3093\u3066\u30bf\u30a4\u30c8\u30eb\u4ed8\u3051\u3066\u308b\u3051\u3069\u5b9f\u306f\u4ed6\u306e\u3084\u308a\u65b9\u3092\u3042\u307e\u308a\u8abf\u3079\u3066\u306a\u3044\u3068\u3044\u3046\u304b\u3001OpenCL\u306f\u3058\u3081\u3066\u6570\u6642\u9593\u306e\u521d\u5fc3\u8005\u306a\u306e\u3067\u3001\u3082\u3063\u3068\u3044\u3044\u65b9\u6cd5\u304c\u3042\u308c\u3070\u6559\u3048\u3066\u304f\u3060\u3055\u3044\u3002<\/p>\n

0. \u6e96\u5099<\/h3>\n

\u4eca\u56de\u4f7f\u3063\u305f\u306e\u306fXcode 4.6.2\u3002
\nCUDA\u306e\u3068\u304d\u306fCUDA\u30c9\u30e9\u30a4\u30d0\u3084toolkit\u306e\u30a4\u30f3\u30b9\u30c8\u30fc\u30eb\u304c\u5fc5\u8981\u3060\u3063\u305f\u3051\u3069\u3001\u6700\u8fd1\u306eMac\u306fOpenCL\u306b\u6a19\u6e96\u5bfe\u5fdc\u3057\u3066\u308b\u306e\u3067Xcode\u3055\u3048\u3042\u308c\u3070\u3059\u3050\u306b\u958b\u767a\u3092\u306f\u3058\u3081\u3089\u308c\u308b\u306f\u305a\u3002<\/p>\n

OpenCL\u306f\u7279\u306bGPU\u9650\u5b9a\u306eAPI\u3063\u3066\u30ef\u30b1\u3058\u3083\u306a\u3044\u3051\u3069\u3001\u4eca\u56de\u306fGPU\u306e\u5229\u7528\u3092\u524d\u63d0\u3068\u3057\u305f\u8aac\u660e\u3068\u306a\u308b\u3002<\/p>\n

1. Xcode\u3067\u65b0\u898f\u30d7\u30ed\u30b8\u30a7\u30af\u30c8\u3092\u4f5c\u6210<\/h3>\n

OS X \u2192 Application \u2192 Command Line Tool \u3092\u9078\u629e\u3002
\n\u4eca\u56de\u306f\u8a00\u8a9e\u3092C++\u3068\u3057\u305f\u3002<\/p>\n

\u3061\u306a\u307f\u306bCUDA\u306e\u3068\u304d\u306f\u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u306e\u8a00\u8a9e\u3092C\u306b\u3057\u305f\u3051\u3069\u3001CUDA\u30ab\u30fc\u30cd\u30eb\u306fC++\u3067\u66f8\u3051\u308b\u3002
\nOpenCL\u3092\u4f7f\u3046\u4eca\u56de\u306f\u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u306e\u8a00\u8a9e\u3092C++\u3068\u3057\u305f\u3051\u3069\u3001OpenCL\u30ab\u30fc\u30cd\u30eb\u306fC\u3067\u66f8\u304f\u5fc5\u8981\u304c\u3042\u308b\u3002
\n\u3064\u307e\u308a\u8a00\u8a9e\u306e\u9078\u629e\u304c\u3042\u3079\u3053\u3079\u306a\u3093\u3060\u3051\u3069\u3001\u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u306e\u8a00\u8a9e\u3092\u81ea\u7531\u306b\u9078\u3079\u308b\u3068\u3044\u3046\u4e8b\u3092\u793a\u3059\u305f\u3081\u306b\u6562\u3048\u3066\u305d\u3046\u3057\u3066\u3044\u308b\u3002<\/p>\n

\u30d7\u30ed\u30b8\u30a7\u30af\u30c8\u540d\u306fOpenCLTest\u3002
\nTERGETS \u2192 Build Phases \u2192 Link Binary With Libraries \u306b\u3066 OpenCL.framework \u3092\u8ffd\u52a0\u3002<\/p>\n

2. \u30ab\u30fc\u30cd\u30eb\u3092\u66f8\u304f<\/h3>\n

kernel.cl \u3068\u3044\u3046\u30d5\u30a1\u30a4\u30eb\u3092\u65b0\u898f\u8ffd\u52a0\u3057\u30b3\u30fc\u30c9\u3092\u66f8\u304f\u3002
\n\u4eca\u56de\u306f\u30c6\u30b9\u30c8\u3068\u3044\u3046\u3053\u3068\u3067\u4ee5\u4e0b\u306e\u3088\u3046\u306b\u30c7\u30fc\u30bf\u3092\u30a4\u30f3\u30af\u30ea\u30e1\u30f3\u30c8\u3059\u308b\u3060\u3051\u306e\u7c21\u5358\u306a\u30ab\u30fc\u30cd\u30eb\u3092\u66f8\u3044\u305f\u3002<\/p>\n

__kernel\r\nvoid addone(__global float* data, const int n)\r\n{\r\n    int index = get_global_id(0);\r\n    \r\n    if (index < n) {\r\n        data[index] += 1.0f;\r\n    }\r\n}<\/pre>\n
CUDA\u306e\u3068\u304d\u306f\u30a4\u30f3\u30c7\u30af\u30b9\u8a08\u7b97\u90e8\u5206\u3092\u3042\u3048\u3066\u6c4e\u7528\u7684\u306b\u66f8\u3044\u305f\u3068\u3044\u3046\u306e\u3082\u3042\u308b\u3051\u3069\u3001OpenCL\u306e\u5834\u5408\u306fget_global_id\u3060\u3051\u3067\u6e08\u3080\u306e\u3067\u305d\u306e\u70b9\u697d\u3002<\/del>
\nget_global_id(0)\u3060\u3051\u3067\u6e08\u3080\u304b\u3069\u3046\u304b\u306f\u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u304b\u3089\u306e\u30ab\u30fc\u30cd\u30eb\u306e\u547c\u3073\u51fa\u3057\u65b9\u306b\u4f9d\u5b58\u3059\u308b\u3002<\/ins><\/p>\n
3. kernel.cl\u3092\u30b3\u30f3\u30d1\u30a4\u30eb\u3059\u308b\u8a2d\u5b9a<\/h3>\n
Xcode\u306fOpenCL\u306b\u5bfe\u5fdc\u3057\u3066\u3044\u308b\u306e\u3067\u3001CUDA\u306e\u6642\u306e\u3088\u3046\u306b\u72ec\u81ea\u306e\u30d3\u30eb\u30c9\u30eb\u30fc\u30eb\u3092\u8ffd\u52a0\u3057\u305f\u308a\u3059\u308b\u5fc5\u8981\u306f\u306a\u3044\u3002
\n\u666e\u901a\u306eC\u306e\u30bd\u30fc\u30b9\u306e\u3088\u3046\u306b\u3001\u5358\u306b TERGETS \u2192 Build Phases \u2192 Compile Souces \u306b kernel.cl \u3092\u8ffd\u52a0\u3059\u308b\u306e\u307f\u3002<\/p>\n
4. \u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u3092\u66f8\u304f\u3002<\/h3>\n
\u3053\u3053\u307e\u3067\u6765\u305f\u3089\u3042\u3068\u306f main.cpp \u3067 #include <OpenCL\/opencl.h> \u3059\u308b\u3060\u3051\u3067OpenCL\u3092\u4f7f\u3063\u305f\u30b3\u30fc\u30c9\u304c\u66f8\u3051\u308b\u3002
\n\u3068\u308a\u3042\u3048\u305a\u4eca\u56de\u306f\u4ee5\u4e0b\u306e\u3088\u3046\u306a\u30b3\u30fc\u30c9\u3092\u66f8\u3044\u305f\u3002
\n\u51e6\u7406\u5185\u5bb9\u3068\u3057\u3066\u306f\u30011000\u8981\u7d20\u306efloat\u306e\u914d\u5217\u306b+1.0\u3059\u308b\u306e\u307f\u3002
\n\u521d\u671f\u5024\u304c0.0\u301c999.0\u306a\u306e\u3067GPU\u3092\u901a\u3057\u305f\u5f8c\u306f1.0\u301c1000.0\u306b\u306a\u308b\u306f\u305a\u3002<\/p>\n
#include <iostream>\r\n#include <vector>\r\n#include <OpenCL\/opencl.h>\r\n\r\n#define PLATFORM_MAX 4\r\n#define DEVICE_MAX 4\r\n\r\n\r\nvoid EC(cl_int result, const char *title)\r\n{\r\n    if (result != CL_SUCCESS) {\r\n        std::cout << "Error: " << title << "(" << result << ")\\n";\r\n    }\r\n}\r\n\r\n\r\ncl_int err = CL_SUCCESS;\r\nvoid EC2(const char *title)\r\n{\r\n    if (err != CL_SUCCESS) {\r\n        std::cout << "Error: " << title << "(" << err << ")\\n";\r\n    }\r\n    err = CL_SUCCESS;\r\n}\r\n\r\n\r\nint main(int argc, const char * argv[])\r\n{\r\n    \/\/ \u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u4e00\u89a7\u3092\u53d6\u5f97\r\n    cl_platform_id platforms[PLATFORM_MAX];\r\n    cl_uint platformCount;\r\n    EC(clGetPlatformIDs(PLATFORM_MAX, platforms, &platformCount), "clGetPlatformIDs");\r\n    if (platformCount == 0) {\r\n        std::cerr << "No platform.\\n";\r\n        return EXIT_FAILURE;\r\n    }\r\n    \r\n    \/\/ \u898b\u3064\u304b\u3063\u305f\u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u306e\u60c5\u5831\u3092\u5370\u5b57\r\n    for (int i = 0; i < platformCount; i++) {\r\n        char vendor[100] = {0};\r\n        char version[100] = {0};\r\n        EC(clGetPlatformInfo(platforms[i], CL_PLATFORM_VENDOR, sizeof(vendor), vendor, nullptr), "clGetPlatformInfo");\r\n        EC(clGetPlatformInfo(platforms[i], CL_PLATFORM_VERSION, sizeof(version), version, nullptr), "clGetPlatformInfo");\r\n        std::cout << "Platform id: " << platforms[i] << ", Vendor: " << vendor << ", Version: " << version << "\\n";\r\n    }\r\n    \r\n    \/\/ \u30c7\u30d0\u30a4\u30b9\u4e00\u89a7\u3092\u53d6\u5f97\r\n    cl_device_id devices[DEVICE_MAX];\r\n    cl_uint deviceCount;\r\n    EC(clGetDeviceIDs(platforms[0], CL_DEVICE_TYPE_GPU, DEVICE_MAX, devices, &deviceCount), "clGetDeviceIDs");\r\n    if (deviceCount == 0) {\r\n        std::cerr << "No device.\\n";\r\n        return EXIT_FAILURE;\r\n    }\r\n    \r\n    \/\/ \u898b\u3064\u304b\u3063\u305f\u30c7\u30d0\u30a4\u30b9\u306e\u60c5\u5831\u3092\u5370\u5b57\r\n    std::cout << deviceCount << " device(s) found.\\n";\r\n    for (int i = 0; i < deviceCount; i++) {\r\n        char name[100] = {0};\r\n        size_t len;\r\n        EC(clGetDeviceInfo(devices[i], CL_DEVICE_NAME, sizeof(name), name, &len), "clGetDeviceInfo");\r\n        std::cout << "Device id: " << i << ", Name: " << name << "\\n";\r\n    }\r\n    \r\n    \/\/ \u30b3\u30f3\u30c6\u30ad\u30b9\u30c8\u306e\u4f5c\u6210\r\n    cl_context ctx = clCreateContext(nullptr, 1, devices, nullptr, nullptr, &err);\r\n    EC2("clCreateContext");\r\n    \r\n    \/\/ \u30b3\u30f3\u30d1\u30a4\u30eb\u6e08\u307fcl\u30d7\u30ed\u30b0\u30e9\u30e0\u306e\u8aad\u307f\u8fbc\u307f\r\n    const char* bitcode_path = "OpenCL\/kernel.cl.gpu_32.bc";\r\n    size_t len = strlen(bitcode_path);\r\n    cl_program program = clCreateProgramWithBinary(ctx, 1, devices, &len, (const unsigned char**)&bitcode_path, nullptr, &err);\r\n    EC2("clCreateProgramWithBinary");\r\n    \r\n    \/\/ \u30d7\u30ed\u30b0\u30e9\u30e0\u306e\u30d3\u30eb\u30c9\r\n    EC(clBuildProgram(program, 1, devices, nullptr, nullptr, nullptr), "clBuildProgram");\r\n    \r\n    \/\/ \u30ab\u30fc\u30cd\u30eb\u306e\u4f5c\u6210\r\n    cl_kernel kernel = clCreateKernel(program, "addone", &err);\r\n    EC2("clCreateKernel");\r\n    \r\n    \/\/ \u30c7\u30fc\u30bf\u3092\u7528\u610f\r\n    int n = 1000;\r\n    std::vector<float> data(n);\r\n    for (int i = 0; i < n; i++) {\r\n        data[i] = float(i);\r\n    }\r\n    \r\n    \/\/ \u30c7\u30d0\u30a4\u30b9\u30e1\u30e2\u30ea\u3092\u78ba\u4fdd\u3057\u3064\u3064\u30c7\u30fc\u30bf\u3092\u30b3\u30d4\u30fc\r\n    cl_mem device_mem = clCreateBuffer(ctx, CL_MEM_READ_WRITE | CL_MEM_COPY_HOST_PTR, sizeof(float) * n, data.data(), &err);\r\n    EC2("clCreateBuffer");\r\n    \r\n    \/\/ \u30ab\u30fc\u30cd\u30eb\u306e\u5f15\u6570\u3092\u30bb\u30c3\u30c8\r\n    EC(clSetKernelArg(kernel, 0, sizeof(cl_mem), &device_mem), "clSetKernelArg");\r\n    EC(clSetKernelArg(kernel, 1, sizeof(int), &n), "clSetKernelArg");\r\n    \r\n    \/\/ \u30b3\u30de\u30f3\u30c9\u30ad\u30e5\u30fc\u306e\u4f5c\u6210\r\n    cl_command_queue q = clCreateCommandQueue(ctx, devices[0], 0, &err);\r\n    EC2("clCreateCommandQueue");\r\n    \r\n    \/\/ \u30ab\u30fc\u30cd\u30eb\u306e\u5b9f\u884c\r\n    size_t global = n;\r\n    EC(clEnqueueNDRangeKernel(q, kernel, 1, nullptr, &global, nullptr, 0, nullptr, nullptr), "clEnqueueNDRangeKernel");\r\n    \r\n    \/\/ \u7d50\u679c\u3092\u8aad\u307f\u8fbc\u307f\r\n    EC(clEnqueueReadBuffer(q, device_mem, CL_TRUE, 0, sizeof(float) * n, data.data(), 0, nullptr, nullptr), "clEnqueueReadBuffer");\r\n    \r\n    \/\/ \u7d50\u679c\u306e\u5370\u5b57\r\n    for (int i = 0; i < n; i++) {\r\n        std::cout << data[i] << ", ";\r\n    }\r\n    std::cout << "\\n";\r\n    \r\n    \/\/ \u30b3\u30de\u30f3\u30c9\u30ad\u30e5\u30fc\u306e\u89e3\u653e\r\n    EC(clReleaseCommandQueue(q), "clReleaseCommandQueue");\r\n    \r\n    \/\/ \u30c7\u30d0\u30a4\u30b9\u30e1\u30e2\u30ea\u3092\u89e3\u653e\r\n    EC(clReleaseMemObject(device_mem), "clReleaseMemObject");\r\n    \r\n    \/\/ \u30ab\u30fc\u30cd\u30eb\u306e\u89e3\u653e\r\n    EC(clReleaseKernel(kernel), "clReleaseKernel");\r\n    \r\n    \/\/ \u30d7\u30ed\u30b0\u30e9\u30e0\u306e\u89e3\u653e\r\n    EC(clReleaseProgram(program), "clReleaseProgram");\r\n    \r\n    \/\/ \u30b3\u30f3\u30c6\u30ad\u30b9\u30c8\u306e\u89e3\u653e\r\n    EC(clReleaseContext(ctx), "clReleaseContext");\r\n    \r\n    std::cout << "Done.\\n";\r\n    return EXIT_SUCCESS;\r\n}<\/pre>\n
\u51e6\u7406\u306e\u6d41\u308c\u306fCUDA Driver API\u306e\u5834\u5408\u3068\u307b\u3068\u3093\u3069\u540c\u3058\u3068\u3044\u3046\u5370\u8c61\u3002<\/p>\n
5. \u5b9f\u884c\u7d50\u679c<\/h3>\n
Platform id: 0x7fff0000, Vendor: Apple, Version: OpenCL 1.2 (Dec  4 2012 18:26:30)\r\n1 device(s) found.\r\nDevice id: 0, Name: GeForce 9400M\r\n1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15, 16, 17, 18, 19, 20, 21, 22, 23, 24, 25, 26, 27, 28, 29, 30, 31, 32, 33, 34, 35, 36, 37, 38, 39, 40, \r\n\u30fc\u30fc\u30fc\u3000\u5927\u80c6\u306b\u7701\u7565\u3000\u30fc\u30fc\u30fc\r\n971, 972, 973, 974, 975, 976, 977, 978, 979, 980, 981, 982, 983, 984, 985, 986, 987, 988, 989, 990, 991, 992, 993, 994, 995, 996, 997, 998, 999, 1000, \r\nDone.<\/pre>\n
6. \u611f\u60f3<\/h3>\n
CUDA Driver API\u3092\u4f7f\u3063\u305f\u7d4c\u9a13\u304c\u3042\u308c\u3070OpenCL\u306f\u305d\u3046\u96e3\u3057\u304f\u306a\u3044\u306e\u3067\u306f\u306a\u3044\u304b\u3068\u3044\u3046\u5370\u8c61\u3092\u53d7\u3051\u305f\u3002
\nOpenCL\u306fCUDA\u3088\u308a\u9762\u5012\u3068\u3044\u3046\u8a71\u306f\u3088\u304f\u805e\u304f\u304c\u3001Driver API\u3070\u3063\u304b\u308a\u4f7f\u3063\u3066\u308b\u8eab\u3068\u3057\u3066\u306f\u3001Xcode\u306e\u30b5\u30dd\u30fc\u30c8\u306e\u304a\u304b\u3052\u3082\u3042\u3063\u3066\u3001OpenCL\u306e\u65b9\u304c\u7c21\u5358\u306b\u611f\u3058\u308b\u3002
\nMac\u306f\u5c11\u3057\u53e4\u304f\u306a\u308b\u3068\u65b0\u3057\u3044GPU\u30c9\u30e9\u30a4\u30d0\u304c\u30a2\u30c3\u30d7\u30c7\u30fc\u30c8\u3067\u914d\u4fe1\u3055\u308c\u306a\u304f\u306a\u308b\u307f\u305f\u3044\u306a\u306e\u3067\u3001CUDA\u3092\u4f7f\u3046\u3088\u308a\u306f\u6a19\u6e96\u5bfe\u5fdc\u306eOpenCL\u3092\u4f7f\u3063\u305f\u307b\u3046\u304c\u3044\u3044\u304b\u3082\u3057\u308c\u306a\u3044\u3002<\/p>\n
\u305f\u3060\u3001OpenGL\u306e\u30b7\u30a7\u30fc\u30c0\u3082\u305d\u3046\u3060\u3051\u3069\u3001GPU\u30e1\u30fc\u30ab\u30fc\u306e\u30c9\u30e9\u30a4\u30d0\u306e\u51fa\u6765\u4e0d\u51fa\u6765\u3067\u3001\u30b3\u30f3\u30d1\u30a4\u30eb\u3057\u305f\u30b7\u30a7\u30fc\u30c0\u3084\u30ab\u30fc\u30cd\u30eb\u306e\u52d5\u304d\u306b\u9055\u3044\u304c\u51fa\u308b\u3089\u3057\u3044\u3068\u3044\u3046\u8a71\u3082\u3042\u308b\u306e\u3067\u6ce8\u610f\u304c\u5fc5\u8981\u3002
\nCUDA\u306e\u307b\u3046\u306fNVIDIA\u9650\u5b9a\u306a\u306e\u3067\u305d\u3046\u3044\u3046\u554f\u984c\u306f\u3042\u307e\u308a\u306a\u3044\u3068\u601d\u308f\u308c\u308b\u3002
\n\uff08\u307e\u3041\u3053\u308c\u306f\u5f53\u305f\u308a\u524d\u3067\u3001\u30e1\u30ea\u30c3\u30c8\u3068\u3044\u3046\u3088\u308a\u30c7\u30e1\u30ea\u30c3\u30c8\u306a\u3093\u3060\u3051\u3069\u3002\uff09<\/p>\n
\u500b\u4eba\u7684\u306b\u306f\u3001\u30ab\u30fc\u30cd\u30eb\u3092C\u3067\u66f8\u304b\u306a\u304d\u3083\u3044\u3051\u306a\u3044\u306e\u304c\u3064\u3089\u3044\u3002
\n\u3084\u3063\u3071\u30af\u30e9\u30b9\u4f7f\u3044\u305f\u3044\u3057\u3002
\nAMD\u306e\u30c4\u30fc\u30eb\u3092\u4f7f\u3063\u305f\u308a\u3001LLVM Clang\u3067\u5de5\u592b\u3059\u308c\u3070C++\u3067\u30ab\u30fc\u30cd\u30eb\u3092\u66f8\u304f\u306e\u3082\u4e0d\u53ef\u80fd\u3067\u306f\u306a\u3044\u3089\u3057\u3044\u3002
\nnvcc\u3068\u6bd4\u3079\u3066\u3069\u306e\u304f\u3089\u3044\u306eC++\u5bfe\u5fdc\u5177\u5408\u304b\u5f8c\u3067\u8abf\u3079\u3066\u307f\u305f\u3044\u3002
\n\u305f\u3060\u3001\u74b0\u5883\u304c\u9650\u3089\u308c\u308b\u306a\u3089\u666e\u901a\u306bCUDA\u4f7f\u3063\u305f\u307b\u3046\u304c\u30de\u30b7\u304b\u3082\u3002<\/ins><\/p>\n
\u3042\u3068\u3001OpenCL\u306e\u95a2\u6570\u306fextern\u3067\u5f15\u6570\u540d\u7121\u3057\u3067\u5ba3\u8a00\u3055\u308c\u3066\u308b\u306e\u3067\u3001Xcode\u306e\u30b3\u30fc\u30c9\u88dc\u5b8c\u6642\u306b\u5f15\u6570\u306e\u578b\u3057\u304b\u51fa\u3066\u3053\u306a\u304f\u3066\u3001\u5177\u4f53\u7684\u306b\u4f55\u3092\u6307\u5b9a\u3059\u308c\u3070\u3044\u3044\u306e\u304b\u304c\u63a8\u6e2c\u3057\u3065\u3089\u3044\u3002
\n\u7d30\u304b\u3044\u70b9\u3060\u3051\u3069\u3053\u308c\u306f\u8a18\u61b6\u529b\u304c\u5f31\u3044\u79c1\u306b\u306f\u5730\u5473\u306b\u3064\u3089\u3044\u3002
\n\u5f8c\u304b\u3089\u77e5\u3063\u305f\u4e8b\u3060\u304c\u3001OpenCL\u306b\u306fopencl.h\u306e\u304b\u308f\u308a\u306bcl.hpp\u3092include\u3059\u308b\u4e8b\u3067\u4f7f\u3048\u308b\u3001C++ Bindings\u3068\u3044\u3046\u3082\u306e\u304c\u3042\u3063\u3066\u3001C++\u3067\u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u3092\u66f8\u304f\u5834\u5408\u306f\u305d\u308c\u3092\u4f7f\u3046\u3068\u3044\u3044\u3089\u3057\u3044\u3002<\/ins><\/p>\n
\u3082\u3046\u3072\u3068\u3064\u3001OpenCL\u306e\u95a2\u6570\u306f\u30a8\u30e9\u30fc\u30b3\u30fc\u30c9\u3092\u8fd4\u308a\u5024\u3067\u8fd4\u3059\u3082\u306e\u3068\u3001\u30dd\u30a4\u30f3\u30bf\u5f15\u6570\u3067\u8fd4\u3059\u3082\u306e\u304c\u6df7\u5728\u3057\u3066\u308b\u306e\u3067\u3001\u5bfe\u5fdc\u3059\u308b\u306e\u304c\u5c11\u3057\u9762\u5012\u304b\u3082\u3057\u308c\u306a\u3044\u3002<\/p>\n
\u500b\u4eba\u3067NVIDIA\u306eGPU\u3092\u4f7f\u3063\u3066GPGPU\u3059\u308b\u5834\u5408\u306fCUDA\u3092\u3001\u914d\u5e03\u3092\u60f3\u5b9a\u3059\u308b\u5834\u5408\u3084\u3001Mac\u3067\u672c\u683c\u7684\u306bGPGPU\u3059\u308b\u5834\u5408\u306fOpenCL\u3092\u9078\u629e\u3059\u308b\u306e\u304c\u826f\u3044\u3093\u3058\u3083\u306a\u3044\u304b\u3068\u601d\u3063\u305f\u3002<\/p>\n","protected":false},"excerpt":{"rendered":"
\u4ee5\u524d\u66f8\u3044\u305fCUDA\u306e\u8a18\u4e8b<\/a>\u306eOpenCL\u7248\u3002
\n\u3053\u3061\u3089\u3082\u3001\u3044\u3061\u3070\u3093\u7c21\u5358\u306a\u3093\u3066\u30bf\u30a4\u30c8\u30eb\u4ed8\u3051\u3066\u308b\u3051\u3069\u5b9f\u306f\u4ed6\u306e\u3084\u308a\u65b9\u3092\u3042\u307e\u308a\u8abf\u3079\u3066\u306a\u3044\u3068\u3044\u3046\u304b\u3001OpenCL\u306f\u3058\u3081\u3066\u6570\u6642\u9593\u306e\u521d\u5fc3\u8005\u306a\u306e\u3067\u3001\u3082\u3063\u3068\u3044\u3044\u65b9\u6cd5\u304c\u3042\u308c\u3070\u6559\u3048\u3066\u304f\u3060\u3055\u3044\u3002<\/p>\n
0. \u6e96\u5099<\/h3>\n
\u4eca\u56de\u4f7f\u3063\u305f\u306e\u306fXcode 4.6.2\u3002
\nCUDA\u306e\u3068\u304d\u306fCUDA\u30c9\u30e9\u30a4\u30d0\u3084toolkit\u306e\u30a4\u30f3\u30b9\u30c8\u30fc\u30eb\u304c\u5fc5\u8981\u3060\u3063\u305f\u3051\u3069\u3001\u6700\u8fd1\u306eMac\u306fOpenCL\u306b\u6a19\u6e96\u5bfe\u5fdc\u3057\u3066\u308b\u306e\u3067Xcode\u3055\u3048\u3042\u308c\u3070\u3059\u3050\u306b\u958b\u767a\u3092\u306f\u3058\u3081\u3089\u308c\u308b\u306f\u305a\u3002<\/p>\n
OpenCL\u306f\u7279\u306bGPU\u9650\u5b9a\u306eAPI\u3063\u3066\u30ef\u30b1\u3058\u3083\u306a\u3044\u3051\u3069\u3001\u4eca\u56de\u306fGPU\u306e\u5229\u7528\u3092\u524d\u63d0\u3068\u3057\u305f\u8aac\u660e\u3068\u306a\u308b\u3002<\/p>\n
1. Xcode\u3067\u65b0\u898f\u30d7\u30ed\u30b8\u30a7\u30af\u30c8\u3092\u4f5c\u6210<\/h3>\n
OS X \u2192 Application \u2192 Command Line Tool \u3092\u9078\u629e\u3002
\n\u4eca\u56de\u306f\u8a00\u8a9e\u3092C++\u3068\u3057\u305f\u3002<\/p>\n
\u3061\u306a\u307f\u306bCUDA\u306e\u3068\u304d\u306f\u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u306e\u8a00\u8a9e\u3092C\u306b\u3057\u305f\u3051\u3069\u3001CUDA\u30ab\u30fc\u30cd\u30eb\u306fC++\u3067\u66f8\u3051\u308b\u3002
\nOpenCL\u3092\u4f7f\u3046\u4eca\u56de\u306f\u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u306e\u8a00\u8a9e\u3092C++\u3068\u3057\u305f\u3051\u3069\u3001OpenCL\u30ab\u30fc\u30cd\u30eb\u306fC\u3067\u66f8\u304f\u5fc5\u8981\u304c\u3042\u308b\u3002
\n\u3064\u307e\u308a\u8a00\u8a9e\u306e\u9078\u629e\u304c\u3042\u3079\u3053\u3079\u306a\u3093\u3060\u3051\u3069\u3001\u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u306e\u8a00\u8a9e\u3092\u81ea\u7531\u306b\u9078\u3079\u308b\u3068\u3044\u3046\u4e8b\u3092\u793a\u3059\u305f\u3081\u306b\u6562\u3048\u3066\u305d\u3046\u3057\u3066\u3044\u308b\u3002<\/p>\n
\u30d7\u30ed\u30b8\u30a7\u30af\u30c8\u540d\u306fOpenCLTest\u3002
\nTERGETS \u2192 Build Phases \u2192 Link Binary With Libraries \u306b\u3066 OpenCL.framework \u3092\u8ffd\u52a0\u3002<\/p>\n
2. \u30ab\u30fc\u30cd\u30eb\u3092\u66f8\u304f<\/h3>\n
kernel.cl \u3068\u3044\u3046\u30d5\u30a1\u30a4\u30eb\u3092\u65b0\u898f\u8ffd\u52a0\u3057\u30b3\u30fc\u30c9\u3092\u66f8\u304f\u3002
\n\u4eca\u56de\u306f\u30c6\u30b9\u30c8\u3068\u3044\u3046\u3053\u3068\u3067\u4ee5\u4e0b\u306e\u3088\u3046\u306b\u30c7\u30fc\u30bf\u3092\u30a4\u30f3\u30af\u30ea\u30e1\u30f3\u30c8\u3059\u308b\u3060\u3051\u306e\u7c21\u5358\u306a\u30ab\u30fc\u30cd\u30eb\u3092\u66f8\u3044\u305f\u3002<\/p>\n
__kernel\r\nvoid addone(__global float* data, const int n)\r\n{\r\n    int index = get_global_id(0);\r\n    \r\n    if (index < n) {\r\n        data[index] += 1.0f;\r\n    }\r\n}<\/pre>\n
CUDA\u306e\u3068\u304d\u306f\u30a4\u30f3\u30c7\u30af\u30b9\u8a08\u7b97\u90e8\u5206\u3092\u3042\u3048\u3066\u6c4e\u7528\u7684\u306b\u66f8\u3044\u305f\u3068\u3044\u3046\u306e\u3082\u3042\u308b\u3051\u3069\u3001OpenCL\u306e\u5834\u5408\u306fget_global_id\u3060\u3051\u3067\u6e08\u3080\u306e\u3067\u305d\u306e\u70b9\u697d\u3002<\/del>
\nget_global_id(0)\u3060\u3051\u3067\u6e08\u3080\u304b\u3069\u3046\u304b\u306f\u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u304b\u3089\u306e\u30ab\u30fc\u30cd\u30eb\u306e\u547c\u3073\u51fa\u3057\u65b9\u306b\u4f9d\u5b58\u3059\u308b\u3002<\/ins><\/p>\n
3. kernel.cl\u3092\u30b3\u30f3\u30d1\u30a4\u30eb\u3059\u308b\u8a2d\u5b9a<\/h3>\n
Xcode\u306fOpenCL\u306b\u5bfe\u5fdc\u3057\u3066\u3044\u308b\u306e\u3067\u3001CUDA\u306e\u6642\u306e\u3088\u3046\u306b\u72ec\u81ea\u306e\u30d3\u30eb\u30c9\u30eb\u30fc\u30eb\u3092\u8ffd\u52a0\u3057\u305f\u308a\u3059\u308b\u5fc5\u8981\u306f\u306a\u3044\u3002
\n\u666e\u901a\u306eC\u306e\u30bd\u30fc\u30b9\u306e\u3088\u3046\u306b\u3001\u5358\u306b TERGETS \u2192 Build Phases \u2192 Compile Souces \u306b kernel.cl \u3092\u8ffd\u52a0\u3059\u308b\u306e\u307f\u3002<\/p>\n
4. \u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u3092\u66f8\u304f\u3002<\/h3>\n
\u3053\u3053\u307e\u3067\u6765\u305f\u3089\u3042\u3068\u306f main.cpp \u3067 #include <OpenCL\/opencl.h> \u3059\u308b\u3060\u3051\u3067OpenCL\u3092\u4f7f\u3063\u305f\u30b3\u30fc\u30c9\u304c\u66f8\u3051\u308b\u3002
\n\u3068\u308a\u3042\u3048\u305a\u4eca\u56de\u306f\u4ee5\u4e0b\u306e\u3088\u3046\u306a\u30b3\u30fc\u30c9\u3092\u66f8\u3044\u305f\u3002
\n\u51e6\u7406\u5185\u5bb9\u3068\u3057\u3066\u306f\u30011000\u8981\u7d20\u306efloat\u306e\u914d\u5217\u306b+1.0\u3059\u308b\u306e\u307f\u3002
\n\u521d\u671f\u5024\u304c0.0\u301c999.0\u306a\u306e\u3067GPU\u3092\u901a\u3057\u305f\u5f8c\u306f1.0\u301c1000.0\u306b\u306a\u308b\u306f\u305a\u3002<\/p>\n
#include <iostream>\r\n#include <vector>\r\n#include <OpenCL\/opencl.h>\r\n\r\n#define PLATFORM_MAX 4\r\n#define DEVICE_MAX 4\r\n\r\n\r\nvoid EC(cl_int result, const char *title)\r\n{\r\n    if (result != CL_SUCCESS) {\r\n        std::cout << "Error: " << title << "(" << result << ")\\n";\r\n    }\r\n}\r\n\r\n\r\ncl_int err = CL_SUCCESS;\r\nvoid EC2(const char *title)\r\n{\r\n    if (err != CL_SUCCESS) {\r\n        std::cout << "Error: " << title << "(" << err << ")\\n";\r\n    }\r\n    err = CL_SUCCESS;\r\n}\r\n\r\n\r\nint main(int argc, const char * argv[])\r\n{\r\n    \/\/ \u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u4e00\u89a7\u3092\u53d6\u5f97\r\n    cl_platform_id platforms[PLATFORM_MAX];\r\n    cl_uint platformCount;\r\n    EC(clGetPlatformIDs(PLATFORM_MAX, platforms, &platformCount), "clGetPlatformIDs");\r\n    if (platformCount == 0) {\r\n        std::cerr << "No platform.\\n";\r\n        return EXIT_FAILURE;\r\n    }\r\n    \r\n    \/\/ \u898b\u3064\u304b\u3063\u305f\u30d7\u30e9\u30c3\u30c8\u30d5\u30a9\u30fc\u30e0\u306e\u60c5\u5831\u3092\u5370\u5b57\r\n    for (int i = 0; i < platformCount; i++) {\r\n        char vendor[100] = {0};\r\n        char version[100] = {0};\r\n        EC(clGetPlatformInfo(platforms[i], CL_PLATFORM_VENDOR, sizeof(vendor), vendor, nullptr), "clGetPlatformInfo");\r\n        EC(clGetPlatformInfo(platforms[i], CL_PLATFORM_VERSION, sizeof(version), version, nullptr), "clGetPlatformInfo");\r\n        std::cout << "Platform id: " << platforms[i] << ", Vendor: " << vendor << ", Version: " << version << "\\n";\r\n    }\r\n    \r\n    \/\/ \u30c7\u30d0\u30a4\u30b9\u4e00\u89a7\u3092\u53d6\u5f97\r\n    cl_device_id devices[DEVICE_MAX];\r\n    cl_uint deviceCount;\r\n    EC(clGetDeviceIDs(platforms[0], CL_DEVICE_TYPE_GPU, DEVICE_MAX, devices, &deviceCount), "clGetDeviceIDs");\r\n    if (deviceCount == 0) {\r\n        std::cerr << "No device.\\n";\r\n        return EXIT_FAILURE;\r\n    }\r\n    \r\n    \/\/ \u898b\u3064\u304b\u3063\u305f\u30c7\u30d0\u30a4\u30b9\u306e\u60c5\u5831\u3092\u5370\u5b57\r\n    std::cout << deviceCount << " device(s) found.\\n";\r\n    for (int i = 0; i < deviceCount; i++) {\r\n        char name[100] = {0};\r\n        size_t len;\r\n        EC(clGetDeviceInfo(devices[i], CL_DEVICE_NAME, sizeof(name), name, &len), "clGetDeviceInfo");\r\n        std::cout << "Device id: " << i << ", Name: " << name << "\\n";\r\n    }\r\n    \r\n    \/\/ \u30b3\u30f3\u30c6\u30ad\u30b9\u30c8\u306e\u4f5c\u6210\r\n    cl_context ctx = clCreateContext(nullptr, 1, devices, nullptr, nullptr, &err);\r\n    EC2("clCreateContext");\r\n    \r\n    \/\/ \u30b3\u30f3\u30d1\u30a4\u30eb\u6e08\u307fcl\u30d7\u30ed\u30b0\u30e9\u30e0\u306e\u8aad\u307f\u8fbc\u307f\r\n    const char* bitcode_path = "OpenCL\/kernel.cl.gpu_32.bc";\r\n    size_t len = strlen(bitcode_path);\r\n    cl_program program = clCreateProgramWithBinary(ctx, 1, devices, &len, (const unsigned char**)&bitcode_path, nullptr, &err);\r\n    EC2("clCreateProgramWithBinary");\r\n    \r\n    \/\/ \u30d7\u30ed\u30b0\u30e9\u30e0\u306e\u30d3\u30eb\u30c9\r\n    EC(clBuildProgram(program, 1, devices, nullptr, nullptr, nullptr), "clBuildProgram");\r\n    \r\n    \/\/ \u30ab\u30fc\u30cd\u30eb\u306e\u4f5c\u6210\r\n    cl_kernel kernel = clCreateKernel(program, "addone", &err);\r\n    EC2("clCreateKernel");\r\n    \r\n    \/\/ \u30c7\u30fc\u30bf\u3092\u7528\u610f\r\n    int n = 1000;\r\n    std::vector<float> data(n);\r\n    for (int i = 0; i < n; i++) {\r\n        data[i] = float(i);\r\n    }\r\n    \r\n    \/\/ \u30c7\u30d0\u30a4\u30b9\u30e1\u30e2\u30ea\u3092\u78ba\u4fdd\u3057\u3064\u3064\u30c7\u30fc\u30bf\u3092\u30b3\u30d4\u30fc\r\n    cl_mem device_mem = clCreateBuffer(ctx, CL_MEM_READ_WRITE | CL_MEM_COPY_HOST_PTR, sizeof(float) * n, data.data(), &err);\r\n    EC2("clCreateBuffer");\r\n    \r\n    \/\/ \u30ab\u30fc\u30cd\u30eb\u306e\u5f15\u6570\u3092\u30bb\u30c3\u30c8\r\n    EC(clSetKernelArg(kernel, 0, sizeof(cl_mem), &device_mem), "clSetKernelArg");\r\n    EC(clSetKernelArg(kernel, 1, sizeof(int), &n), "clSetKernelArg");\r\n    \r\n    \/\/ \u30b3\u30de\u30f3\u30c9\u30ad\u30e5\u30fc\u306e\u4f5c\u6210\r\n    cl_command_queue q = clCreateCommandQueue(ctx, devices[0], 0, &err);\r\n    EC2("clCreateCommandQueue");\r\n    \r\n    \/\/ \u30ab\u30fc\u30cd\u30eb\u306e\u5b9f\u884c\r\n    size_t global = n;\r\n    EC(clEnqueueNDRangeKernel(q, kernel, 1, nullptr, &global, nullptr, 0, nullptr, nullptr), "clEnqueueNDRangeKernel");\r\n    \r\n    \/\/ \u7d50\u679c\u3092\u8aad\u307f\u8fbc\u307f\r\n    EC(clEnqueueReadBuffer(q, device_mem, CL_TRUE, 0, sizeof(float) * n, data.data(), 0, nullptr, nullptr), "clEnqueueReadBuffer");\r\n    \r\n    \/\/ \u7d50\u679c\u306e\u5370\u5b57\r\n    for (int i = 0; i < n; i++) {\r\n        std::cout << data[i] << ", ";\r\n    }\r\n    std::cout << "\\n";\r\n    \r\n    \/\/ \u30b3\u30de\u30f3\u30c9\u30ad\u30e5\u30fc\u306e\u89e3\u653e\r\n    EC(clReleaseCommandQueue(q), "clReleaseCommandQueue");\r\n    \r\n    \/\/ \u30c7\u30d0\u30a4\u30b9\u30e1\u30e2\u30ea\u3092\u89e3\u653e\r\n    EC(clReleaseMemObject(device_mem), "clReleaseMemObject");\r\n    \r\n    \/\/ \u30ab\u30fc\u30cd\u30eb\u306e\u89e3\u653e\r\n    EC(clReleaseKernel(kernel), "clReleaseKernel");\r\n    \r\n    \/\/ \u30d7\u30ed\u30b0\u30e9\u30e0\u306e\u89e3\u653e\r\n    EC(clReleaseProgram(program), "clReleaseProgram");\r\n    \r\n    \/\/ \u30b3\u30f3\u30c6\u30ad\u30b9\u30c8\u306e\u89e3\u653e\r\n    EC(clReleaseContext(ctx), "clReleaseContext");\r\n    \r\n    std::cout << "Done.\\n";\r\n    return EXIT_SUCCESS;\r\n}<\/pre>\n
\u51e6\u7406\u306e\u6d41\u308c\u306fCUDA Driver API\u306e\u5834\u5408\u3068\u307b\u3068\u3093\u3069\u540c\u3058\u3068\u3044\u3046\u5370\u8c61\u3002<\/p>\n
5. \u5b9f\u884c\u7d50\u679c<\/h3>\n
Platform id: 0x7fff0000, Vendor: Apple, Version: OpenCL 1.2 (Dec  4 2012 18:26:30)\r\n1 device(s) found.\r\nDevice id: 0, Name: GeForce 9400M\r\n1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15, 16, 17, 18, 19, 20, 21, 22, 23, 24, 25, 26, 27, 28, 29, 30, 31, 32, 33, 34, 35, 36, 37, 38, 39, 40, \r\n\u30fc\u30fc\u30fc\u3000\u5927\u80c6\u306b\u7701\u7565\u3000\u30fc\u30fc\u30fc\r\n971, 972, 973, 974, 975, 976, 977, 978, 979, 980, 981, 982, 983, 984, 985, 986, 987, 988, 989, 990, 991, 992, 993, 994, 995, 996, 997, 998, 999, 1000, \r\nDone.<\/pre>\n
6. \u611f\u60f3<\/h3>\n
CUDA Driver API\u3092\u4f7f\u3063\u305f\u7d4c\u9a13\u304c\u3042\u308c\u3070OpenCL\u306f\u305d\u3046\u96e3\u3057\u304f\u306a\u3044\u306e\u3067\u306f\u306a\u3044\u304b\u3068\u3044\u3046\u5370\u8c61\u3092\u53d7\u3051\u305f\u3002
\nOpenCL\u306fCUDA\u3088\u308a\u9762\u5012\u3068\u3044\u3046\u8a71\u306f\u3088\u304f\u805e\u304f\u304c\u3001Driver API\u3070\u3063\u304b\u308a\u4f7f\u3063\u3066\u308b\u8eab\u3068\u3057\u3066\u306f\u3001Xcode\u306e\u30b5\u30dd\u30fc\u30c8\u306e\u304a\u304b\u3052\u3082\u3042\u3063\u3066\u3001OpenCL\u306e\u65b9\u304c\u7c21\u5358\u306b\u611f\u3058\u308b\u3002
\nMac\u306f\u5c11\u3057\u53e4\u304f\u306a\u308b\u3068\u65b0\u3057\u3044GPU\u30c9\u30e9\u30a4\u30d0\u304c\u30a2\u30c3\u30d7\u30c7\u30fc\u30c8\u3067\u914d\u4fe1\u3055\u308c\u306a\u304f\u306a\u308b\u307f\u305f\u3044\u306a\u306e\u3067\u3001CUDA\u3092\u4f7f\u3046\u3088\u308a\u306f\u6a19\u6e96\u5bfe\u5fdc\u306eOpenCL\u3092\u4f7f\u3063\u305f\u307b\u3046\u304c\u3044\u3044\u304b\u3082\u3057\u308c\u306a\u3044\u3002<\/p>\n
\u305f\u3060\u3001OpenGL\u306e\u30b7\u30a7\u30fc\u30c0\u3082\u305d\u3046\u3060\u3051\u3069\u3001GPU\u30e1\u30fc\u30ab\u30fc\u306e\u30c9\u30e9\u30a4\u30d0\u306e\u51fa\u6765\u4e0d\u51fa\u6765\u3067\u3001\u30b3\u30f3\u30d1\u30a4\u30eb\u3057\u305f\u30b7\u30a7\u30fc\u30c0\u3084\u30ab\u30fc\u30cd\u30eb\u306e\u52d5\u304d\u306b\u9055\u3044\u304c\u51fa\u308b\u3089\u3057\u3044\u3068\u3044\u3046\u8a71\u3082\u3042\u308b\u306e\u3067\u6ce8\u610f\u304c\u5fc5\u8981\u3002
\nCUDA\u306e\u307b\u3046\u306fNVIDIA\u9650\u5b9a\u306a\u306e\u3067\u305d\u3046\u3044\u3046\u554f\u984c\u306f\u3042\u307e\u308a\u306a\u3044\u3068\u601d\u308f\u308c\u308b\u3002
\n\uff08\u307e\u3041\u3053\u308c\u306f\u5f53\u305f\u308a\u524d\u3067\u3001\u30e1\u30ea\u30c3\u30c8\u3068\u3044\u3046\u3088\u308a\u30c7\u30e1\u30ea\u30c3\u30c8\u306a\u3093\u3060\u3051\u3069\u3002\uff09<\/p>\n
\u500b\u4eba\u7684\u306b\u306f\u3001\u30ab\u30fc\u30cd\u30eb\u3092C\u3067\u66f8\u304b\u306a\u304d\u3083\u3044\u3051\u306a\u3044\u306e\u304c\u3064\u3089\u3044\u3002
\n\u3084\u3063\u3071\u30af\u30e9\u30b9\u4f7f\u3044\u305f\u3044\u3057\u3002
\nAMD\u306e\u30c4\u30fc\u30eb\u3092\u4f7f\u3063\u305f\u308a\u3001LLVM Clang\u3067\u5de5\u592b\u3059\u308c\u3070C++\u3067\u30ab\u30fc\u30cd\u30eb\u3092\u66f8\u304f\u306e\u3082\u4e0d\u53ef\u80fd\u3067\u306f\u306a\u3044\u3089\u3057\u3044\u3002
\nnvcc\u3068\u6bd4\u3079\u3066\u3069\u306e\u304f\u3089\u3044\u306eC++\u5bfe\u5fdc\u5177\u5408\u304b\u5f8c\u3067\u8abf\u3079\u3066\u307f\u305f\u3044\u3002
\n\u305f\u3060\u3001\u74b0\u5883\u304c\u9650\u3089\u308c\u308b\u306a\u3089\u666e\u901a\u306bCUDA\u4f7f\u3063\u305f\u307b\u3046\u304c\u30de\u30b7\u304b\u3082\u3002<\/ins><\/p>\n
\u3042\u3068\u3001OpenCL\u306e\u95a2\u6570\u306fextern\u3067\u5f15\u6570\u540d\u7121\u3057\u3067\u5ba3\u8a00\u3055\u308c\u3066\u308b\u306e\u3067\u3001Xcode\u306e\u30b3\u30fc\u30c9\u88dc\u5b8c\u6642\u306b\u5f15\u6570\u306e\u578b\u3057\u304b\u51fa\u3066\u3053\u306a\u304f\u3066\u3001\u5177\u4f53\u7684\u306b\u4f55\u3092\u6307\u5b9a\u3059\u308c\u3070\u3044\u3044\u306e\u304b\u304c\u63a8\u6e2c\u3057\u3065\u3089\u3044\u3002
\n\u7d30\u304b\u3044\u70b9\u3060\u3051\u3069\u3053\u308c\u306f\u8a18\u61b6\u529b\u304c\u5f31\u3044\u79c1\u306b\u306f\u5730\u5473\u306b\u3064\u3089\u3044\u3002
\n\u5f8c\u304b\u3089\u77e5\u3063\u305f\u4e8b\u3060\u304c\u3001OpenCL\u306b\u306fopencl.h\u306e\u304b\u308f\u308a\u306bcl.hpp\u3092include\u3059\u308b\u4e8b\u3067\u4f7f\u3048\u308b\u3001C++ Bindings\u3068\u3044\u3046\u3082\u306e\u304c\u3042\u3063\u3066\u3001C++\u3067\u30db\u30b9\u30c8\u30b3\u30fc\u30c9\u3092\u66f8\u304f\u5834\u5408\u306f\u305d\u308c\u3092\u4f7f\u3046\u3068\u3044\u3044\u3089\u3057\u3044\u3002<\/ins><\/p>\n
\u3082\u3046\u3072\u3068\u3064\u3001OpenCL\u306e\u95a2\u6570\u306f\u30a8\u30e9\u30fc\u30b3\u30fc\u30c9\u3092\u8fd4\u308a\u5024\u3067\u8fd4\u3059\u3082\u306e\u3068\u3001\u30dd\u30a4\u30f3\u30bf\u5f15\u6570\u3067\u8fd4\u3059\u3082\u306e\u304c\u6df7\u5728\u3057\u3066\u308b\u306e\u3067\u3001\u5bfe\u5fdc\u3059\u308b\u306e\u304c\u5c11\u3057\u9762\u5012\u304b\u3082\u3057\u308c\u306a\u3044\u3002<\/p>\n
\u500b\u4eba\u3067NVIDIA\u306eGPU\u3092\u4f7f\u3063\u3066GPGPU\u3059\u308b\u5834\u5408\u306fCUDA\u3092\u3001\u914d\u5e03\u3092\u60f3\u5b9a\u3059\u308b\u5834\u5408\u3084\u3001Mac\u3067\u672c\u683c\u7684\u306bGPGPU\u3059\u308b\u5834\u5408\u306fOpenCL\u3092\u9078\u629e\u3059\u308b\u306e\u304c\u826f\u3044\u3093\u3058\u3083\u306a\u3044\u304b\u3068\u601d\u3063\u305f\u3002<\/p>\n","protected":false},"author":1,"featured_media":0,"comment_status":"open","ping_status":"open","sticky":false,"template":"","format":"standard","meta":{"footnotes":""},"categories":[32],"tags":[456],"class_list":["post-2538","post","type-post","status-publish","format-standard","hentry","category-tech","tag-opencl"],"_links":{"self":[{"href":"https:\/\/peta.okechan.net\/blog\/wp-json\/wp\/v2\/posts\/2538","targetHints":{"allow":["GET"]}}],"collection":[{"href":"https:\/\/peta.okechan.net\/blog\/wp-json\/wp\/v2\/posts"}],"about":[{"href":"https:\/\/peta.okechan.net\/blog\/wp-json\/wp\/v2\/types\/post"}],"author":[{"embeddable":true,"href":"https:\/\/peta.okechan.net\/blog\/wp-json\/wp\/v2\/users\/1"}],"replies":[{"embeddable":true,"href":"https:\/\/peta.okechan.net\/blog\/wp-json\/wp\/v2\/comments?post=2538"}],"version-history":[{"count":0,"href":"https:\/\/peta.okechan.net\/blog\/wp-json\/wp\/v2\/posts\/2538\/revisions"}],"wp:attachment":[{"href":"https:\/\/peta.okechan.net\/blog\/wp-json\/wp\/v2\/media?parent=2538"}],"wp:term":[{"taxonomy":"category","embeddable":true,"href":"https:\/\/peta.okechan.net\/blog\/wp-json\/wp\/v2\/categories?post=2538"},{"taxonomy":"post_tag","embeddable":true,"href":"https:\/\/peta.okechan.net\/blog\/wp-json\/wp\/v2\/tags?post=2538"}],"curies":[{"name":"wp","href":"https:\/\/api.w.org\/{rel}","templated":true}]}}