Attachment 133257 Details for Bug 102049 – Test case

Test case

testcase.c (text/x-csrc), 11.30 KB, created by Chris Cummins on 2017-08-05 15:30:30 UTC

(hide)

Description:

Filename:

MIME Type:

Creator: Chris Cummins

Created: 2017-08-05 15:30:30 UTC

Size: 11.30 KB

patch

obsolete

>/*
> * Usage: gcc -DPLATFORM_ID=0 -DDEVICE_ID=0 code.c -lOpenCL; ./a.out
> */
>#ifndef PLATFORM_ID
># define PLATFORM_ID 1
>#endif
>
>#ifndef DEVICE_ID
># define DEVICE_ID 0
>#endif
>
>#include <stdio.h>
>#include <stdlib.h>
>
>#ifdef __APPLE__
>#include <OpenCL/opencl.h>
>#else
>#include <CL/cl.h>
>#endif
>
>typedef unsigned char bool;
>
>const char *kernel_src = \
>"__kernel void A(__global float* b, __global float* c, const int d) {\n"
>"  int e = get_global_id(0);\n"
>"  b[e] = (char)(c[e] + d);\n"
>"}\n";
>
>const char *clerror_string(cl_int err) {
>    /* written by @Selmar http://stackoverflow.com/a/24336429 */
>    switch(err) {
>        /* run-time and JIT compiler errors */
>        case 0: return "CL_SUCCESS";
>        case -1: return "CL_DEVICE_NOT_FOUND";
>        case -2: return "CL_DEVICE_NOT_AVAILABLE";
>        case -3: return "CL_COMPILER_NOT_AVAILABLE";
>        case -4: return "CL_MEM_OBJECT_ALLOCATION_FAILURE";
>        case -5: return "CL_OUT_OF_RESOURCES";
>        case -6: return "CL_OUT_OF_HOST_MEMORY";
>        case -7: return "CL_PROFILING_INFO_NOT_AVAILABLE";
>        case -8: return "CL_MEM_COPY_OVERLAP";
>        case -9: return "CL_IMAGE_FORMAT_MISMATCH";
>        case -10: return "CL_IMAGE_FORMAT_NOT_SUPPORTED";
>        case -11: return "CL_BUILD_PROGRAM_FAILURE";
>        case -12: return "CL_MAP_FAILURE";
>        case -13: return "CL_MISALIGNED_SUB_BUFFER_OFFSET";
>        case -14: return "CL_EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST";
>        case -15: return "CL_COMPILE_PROGRAM_FAILURE";
>        case -16: return "CL_LINKER_NOT_AVAILABLE";
>        case -17: return "CL_LINK_PROGRAM_FAILURE";
>        case -18: return "CL_DEVICE_PARTITION_FAILED";
>        case -19: return "CL_KERNEL_ARG_INFO_NOT_AVAILABLE";
>
>        /* compile-time errors */
>        case -30: return "CL_INVALID_VALUE";
>        case -31: return "CL_INVALID_DEVICE_TYPE";
>        case -32: return "CL_INVALID_PLATFORM";
>        case -33: return "CL_INVALID_DEVICE";
>        case -34: return "CL_INVALID_CONTEXT";
>        case -35: return "CL_INVALID_QUEUE_PROPERTIES";
>        case -36: return "CL_INVALID_COMMAND_QUEUE";
>        case -37: return "CL_INVALID_HOST_PTR";
>        case -38: return "CL_INVALID_MEM_OBJECT";
>        case -39: return "CL_INVALID_IMAGE_FORMAT_DESCRIPTOR";
>        case -40: return "CL_INVALID_IMAGE_SIZE";
>        case -41: return "CL_INVALID_SAMPLER";
>        case -42: return "CL_INVALID_BINARY";
>        case -43: return "CL_INVALID_BUILD_OPTIONS";
>        case -44: return "CL_INVALID_PROGRAM";
>        case -45: return "CL_INVALID_PROGRAM_EXECUTABLE";
>        case -46: return "CL_INVALID_KERNEL_NAME";
>        case -47: return "CL_INVALID_KERNEL_DEFINITION";
>        case -48: return "CL_INVALID_KERNEL";
>        case -49: return "CL_INVALID_ARG_INDEX";
>        case -50: return "CL_INVALID_ARG_VALUE";
>        case -51: return "CL_INVALID_ARG_SIZE";
>        case -52: return "CL_INVALID_KERNEL_ARGS";
>        case -53: return "CL_INVALID_WORK_DIMENSION";
>        case -54: return "CL_INVALID_WORK_GROUP_SIZE";
>        case -55: return "CL_INVALID_WORK_ITEM_SIZE";
>        case -56: return "CL_INVALID_GLOBAL_OFFSET";
>        case -57: return "CL_INVALID_EVENT_WAIT_LIST";
>        case -58: return "CL_INVALID_EVENT";
>        case -59: return "CL_INVALID_OPERATION";
>        case -60: return "CL_INVALID_GL_OBJECT";
>        case -61: return "CL_INVALID_BUFFER_SIZE";
>        case -62: return "CL_INVALID_MIP_LEVEL";
>        case -63: return "CL_INVALID_GLOBAL_WORK_SIZE";
>        case -64: return "CL_INVALID_PROPERTY";
>        case -65: return "CL_INVALID_IMAGE_DESCRIPTOR";
>        case -66: return "CL_INVALID_COMPILER_OPTIONS";
>        case -67: return "CL_INVALID_LINKER_OPTIONS";
>        case -68: return "CL_INVALID_DEVICE_PARTITION_COUNT";
>
>        /* extension errors */
>        case -1000: return "CL_INVALID_GL_SHAREGROUP_REFERENCE_KHR";
>        case -1001: return "CL_PLATFORM_NOT_FOUND_KHR";
>        case -1002: return "CL_INVALID_D3D10_DEVICE_KHR";
>        case -1003: return "CL_INVALID_D3D10_RESOURCE_KHR";
>        case -1004: return "CL_D3D10_RESOURCE_ALREADY_ACQUIRED_KHR";
>        case -1005: return "CL_D3D10_RESOURCE_NOT_ACQUIRED_KHR";
>
>        default: return "Unknown OpenCL error";
>    }
>}
>
>void check_error(const char* api_call, cl_int err) {
>    if(err != CL_SUCCESS) {
>        fprintf(stderr, "%s %s\n", api_call, clerror_string(err));
>        exit(1);
>    }
>}
>
>int main() {
>    int err;
>
>    cl_uint num_platforms;
>    cl_platform_id *platform_ids = (cl_platform_id*)malloc(sizeof(cl_platform_id) * (PLATFORM_ID + 1));
>    err = clGetPlatformIDs(PLATFORM_ID + 1, platform_ids, &num_platforms);
>    check_error("clGetPlatformIDs", err);
>
>    if (num_platforms <= PLATFORM_ID) {
>        fprintf(stderr, "Platform ID %d not found\n", PLATFORM_ID);
>        return 1;
>    }
>    cl_platform_id platform_id = platform_ids[PLATFORM_ID];
>
>    char strbuf[256];
>    err = clGetPlatformInfo(platform_id, CL_PLATFORM_NAME, sizeof(strbuf), strbuf, NULL);
>    check_error("clGetPlatformInfo", err);
>    fprintf(stderr, "[cldrive] Platform: %s\n", strbuf);
>
>    cl_uint num_devices;
>    cl_device_id *device_ids = (cl_device_id*)malloc(sizeof(cl_device_id) * (DEVICE_ID + 1));
>    err = clGetDeviceIDs(platform_id, CL_DEVICE_TYPE_ALL, DEVICE_ID + 1, device_ids, &num_devices);
>    check_error("clGetDeviceIDs", err);
>
>    if (num_devices <= DEVICE_ID) {
>        fprintf(stderr, "Device ID %d not found\n", DEVICE_ID);
>        return 1;
>    }
>    cl_device_id device_id = device_ids[DEVICE_ID];
>
>    err = clGetDeviceInfo(device_id, CL_DEVICE_NAME, sizeof(strbuf), strbuf, NULL);
>    check_error("clGetDeviceInfo", err);
>    fprintf(stderr, "[cldrive] Device: %s\n", strbuf);
>
>    cl_context ctx = clCreateContext(NULL, 1, &device_id, NULL, NULL, &err);
>    check_error("clCreateContext", err);
>
>    cl_command_queue queue = clCreateCommandQueue(ctx, device_id, 0, &err);
>    check_error("clCreateCommandQueue", err);
>
>    fprintf(stderr, "[cldrive] OpenCL optimizations: off\n");
>
>    cl_program program = clCreateProgramWithSource(ctx, 1, (const char **) &kernel_src, NULL, &err);
>    check_error("clCreateProgramWithSource", err);
>
>    int build_err = clBuildProgram(program, 0, NULL, NULL, NULL, NULL);
>
>    size_t log_size;
>    err = clGetProgramBuildInfo(program, device_id, CL_PROGRAM_BUILD_LOG, 0, NULL, &log_size);
>    check_error("clGetProgramBuildInfo", err);
>
>    if (log_size > 2) {
>        char* log = (char*)malloc(sizeof(char) * (log_size + 1));
>        err = clGetProgramBuildInfo(program, device_id, CL_PROGRAM_BUILD_LOG, log_size, log, NULL);
>        check_error("clGetProgramBuildInfo", err);
>        fprintf(stderr, "%s", log);
>    }
>
>    check_error("clBuildProgram", build_err);
>
>    fprintf(stderr, "[cldrive] Kernel: \"A\"\n");
>    cl_kernel kernel = clCreateKernel(program, "A", &err);
>    check_error("clCreateKernel", err);
>
>    float host_1[256] = { 0.0, 1.0, 2.0, 3.0, 4.0, 5.0, 6.0, 7.0, 8.0, 9.0, 10.0, 11.0, 12.0, 13.0, 14.0, 15.0, 16.0, 17.0, 18.0, 19.0, 20.0, 21.0, 22.0, 23.0, 24.0, 25.0, 26.0, 27.0, 28.0, 29.0, 30.0, 31.0, 32.0, 33.0, 34.0, 35.0, 36.0, 37.0, 38.0, 39.0, 40.0, 41.0, 42.0, 43.0, 44.0, 45.0, 46.0, 47.0, 48.0, 49.0, 50.0, 51.0, 52.0, 53.0, 54.0, 55.0, 56.0, 57.0, 58.0, 59.0, 60.0, 61.0, 62.0, 63.0, 64.0, 65.0, 66.0, 67.0, 68.0, 69.0, 70.0, 71.0, 72.0, 73.0, 74.0, 75.0, 76.0, 77.0, 78.0, 79.0, 80.0, 81.0, 82.0, 83.0, 84.0, 85.0, 86.0, 87.0, 88.0, 89.0, 90.0, 91.0, 92.0, 93.0, 94.0, 95.0, 96.0, 97.0, 98.0, 99.0, 100.0, 101.0, 102.0, 103.0, 104.0, 105.0, 106.0, 107.0, 108.0, 109.0, 110.0, 111.0, 112.0, 113.0, 114.0, 115.0, 116.0, 117.0, 118.0, 119.0, 120.0, 121.0, 122.0, 123.0, 124.0, 125.0, 126.0, 127.0, 128.0, 129.0, 130.0, 131.0, 132.0, 133.0, 134.0, 135.0, 136.0, 137.0, 138.0, 139.0, 140.0, 141.0, 142.0, 143.0, 144.0, 145.0, 146.0, 147.0, 148.0, 149.0, 150.0, 151.0, 152.0, 153.0, 154.0, 155.0, 156.0, 157.0, 158.0, 159.0, 160.0, 161.0, 162.0, 163.0, 164.0, 165.0, 166.0, 167.0, 168.0, 169.0, 170.0, 171.0, 172.0, 173.0, 174.0, 175.0, 176.0, 177.0, 178.0, 179.0, 180.0, 181.0, 182.0, 183.0, 184.0, 185.0, 186.0, 187.0, 188.0, 189.0, 190.0, 191.0, 192.0, 193.0, 194.0, 195.0, 196.0, 197.0, 198.0, 199.0, 200.0, 201.0, 202.0, 203.0, 204.0, 205.0, 206.0, 207.0, 208.0, 209.0, 210.0, 211.0, 212.0, 213.0, 214.0, 215.0, 216.0, 217.0, 218.0, 219.0, 220.0, 221.0, 222.0, 223.0, 224.0, 225.0, 226.0, 227.0, 228.0, 229.0, 230.0, 231.0, 232.0, 233.0, 234.0, 235.0, 236.0, 237.0, 238.0, 239.0, 240.0, 241.0, 242.0, 243.0, 244.0, 245.0, 246.0, 247.0, 248.0, 249.0, 250.0, 251.0, 252.0, 253.0, 254.0, 255.0 };
>    cl_mem dev_1 = clCreateBuffer(ctx, CL_MEM_COPY_HOST_PTR | CL_MEM_READ_WRITE, sizeof(float) * 256, &host_1, &err);
>    check_error("clCreateBuffer", err);
>    err = clSetKernelArg(kernel, 0, sizeof(cl_mem), &dev_1);
>    check_error("clSetKernelArg", err);
>
>    float host_2[256] = { 0.0, 1.0, 2.0, 3.0, 4.0, 5.0, 6.0, 7.0, 8.0, 9.0, 10.0, 11.0, 12.0, 13.0, 14.0, 15.0, 16.0, 17.0, 18.0, 19.0, 20.0, 21.0, 22.0, 23.0, 24.0, 25.0, 26.0, 27.0, 28.0, 29.0, 30.0, 31.0, 32.0, 33.0, 34.0, 35.0, 36.0, 37.0, 38.0, 39.0, 40.0, 41.0, 42.0, 43.0, 44.0, 45.0, 46.0, 47.0, 48.0, 49.0, 50.0, 51.0, 52.0, 53.0, 54.0, 55.0, 56.0, 57.0, 58.0, 59.0, 60.0, 61.0, 62.0, 63.0, 64.0, 65.0, 66.0, 67.0, 68.0, 69.0, 70.0, 71.0, 72.0, 73.0, 74.0, 75.0, 76.0, 77.0, 78.0, 79.0, 80.0, 81.0, 82.0, 83.0, 84.0, 85.0, 86.0, 87.0, 88.0, 89.0, 90.0, 91.0, 92.0, 93.0, 94.0, 95.0, 96.0, 97.0, 98.0, 99.0, 100.0, 101.0, 102.0, 103.0, 104.0, 105.0, 106.0, 107.0, 108.0, 109.0, 110.0, 111.0, 112.0, 113.0, 114.0, 115.0, 116.0, 117.0, 118.0, 119.0, 120.0, 121.0, 122.0, 123.0, 124.0, 125.0, 126.0, 127.0, 128.0, 129.0, 130.0, 131.0, 132.0, 133.0, 134.0, 135.0, 136.0, 137.0, 138.0, 139.0, 140.0, 141.0, 142.0, 143.0, 144.0, 145.0, 146.0, 147.0, 148.0, 149.0, 150.0, 151.0, 152.0, 153.0, 154.0, 155.0, 156.0, 157.0, 158.0, 159.0, 160.0, 161.0, 162.0, 163.0, 164.0, 165.0, 166.0, 167.0, 168.0, 169.0, 170.0, 171.0, 172.0, 173.0, 174.0, 175.0, 176.0, 177.0, 178.0, 179.0, 180.0, 181.0, 182.0, 183.0, 184.0, 185.0, 186.0, 187.0, 188.0, 189.0, 190.0, 191.0, 192.0, 193.0, 194.0, 195.0, 196.0, 197.0, 198.0, 199.0, 200.0, 201.0, 202.0, 203.0, 204.0, 205.0, 206.0, 207.0, 208.0, 209.0, 210.0, 211.0, 212.0, 213.0, 214.0, 215.0, 216.0, 217.0, 218.0, 219.0, 220.0, 221.0, 222.0, 223.0, 224.0, 225.0, 226.0, 227.0, 228.0, 229.0, 230.0, 231.0, 232.0, 233.0, 234.0, 235.0, 236.0, 237.0, 238.0, 239.0, 240.0, 241.0, 242.0, 243.0, 244.0, 245.0, 246.0, 247.0, 248.0, 249.0, 250.0, 251.0, 252.0, 253.0, 254.0, 255.0 };
>    cl_mem dev_2 = clCreateBuffer(ctx, CL_MEM_COPY_HOST_PTR | CL_MEM_READ_WRITE, sizeof(float) * 256, &host_2, &err);
>    check_error("clCreateBuffer", err);
>    err = clSetKernelArg(kernel, 1, sizeof(cl_mem), &dev_2);
>    check_error("clSetKernelArg", err);
>
>    int host_3 = 256;
>    err = clSetKernelArg(kernel, 2, sizeof(int), &host_3);
>    check_error("clSetKernelArg", err);
>
>    const size_t lsize[3] = { 1, 1, 1 };
>    const size_t gsize[3] = { 1, 1, 1 };
>
>    err = clEnqueueNDRangeKernel(queue, kernel, 3, NULL, gsize, lsize, 0, NULL, NULL);
>    check_error("clEnqueueNDRangeKernel", err);
>
>    clEnqueueReadBuffer(queue, dev_1, CL_TRUE, 0, sizeof(float) * 256, &host_1, 0, NULL, NULL);
>
>    err = clFinish(queue);
>    check_error("clFinish", err);
>
>    printf("computed result: %.1f\n", host_1[0]);
>
>    /* clReleaseMemObject(); */
>    clReleaseProgram(program);
>    clReleaseKernel(kernel);
>    clReleaseCommandQueue(queue);
>    clReleaseContext(ctx);
>
>    fprintf(stderr, "done.\n");
>    return 0;
>}

Actions: View

Attachments on bug 102049: 133257

Use of freedesktop.org services, including Bugzilla, is subject to our Code of Conduct. How we collect and use information is described in our Privacy Policy.