Page 3 of 3 FirstFirst 123
Results 21 to 24 of 24

Thread: AMD Radeon R600 GPU LLVM 3.3 Back-End Testing

  1. #21
    Join Date
    May 2011
    Posts
    33

    Default

    Quote Originally Posted by jasn View Post
    So I just now performed a git clone of the opencl-example repository. Next thing is make. Here's that output;

    I believe that this tree does include the "Add clFinish() call to clSimpleEnqueueNDRangeKernel" commit, I'm just not sure what's causing the other fails.

    Thanks..

    Jason
    Looks like I missed a few places that need to call clFinish(). I've pushed a fix to my opencl-example repo. Can you try again?

  2. #22
    Join Date
    Apr 2010
    Posts
    13

    Default

    Tom,

    Everything works perfectly now.
    Code:
    make
    cc -g   -c -o hello_world.o hello_world.c
    cc -g   -c -o cl_simple.o cl_simple.c
    cl_simple.c: In function 'clSimpleCreateBuffer':
    cl_simple.c:80:24: warning: format '%u' expects argument of type 'unsigned int', but argument 5 has type 'cl_mem_flags' [-Wformat]
    cl_simple.c:80:24: warning: format '%u' expects argument of type 'unsigned int', but argument 6 has type 'size_t' [-Wformat]
    cc -g   -c -o cl_util.o cl_util.c
    gcc -o hello_world hello_world.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    cc -g   -c -o math-int.o math-int.c
    gcc -o math-int math-int.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    cc -g   -c -o get_global_id.o get_global_id.c
    gcc -o get-global-id get_global_id.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    cc -g   -c -o get_global_id_2d.o get_global_id_2d.c
    gcc -o get-global-id-2d get_global_id_2d.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    cc -g   -c -o loop.o loop.c
    gcc -o loop loop.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    cc -g   -c -o get_global_id_3d.o get_global_id_3d.c
    get_global_id_3d.c: In function 'main':
    get_global_id_3d.c:36:38: warning: passing argument 4 of 'clSimpleEnqueueNDRangeKernel' from incompatible pointer type [enabled by default]
    In file included from get_global_id_3d.c:6:0:
    cl_simple.h:19:10: note: expected 'const size_t *' but argument is of type 'size_t (*)[3]'
    get_global_id_3d.c:36:38: warning: passing argument 5 of 'clSimpleEnqueueNDRangeKernel' from incompatible pointer type [enabled by default]
    In file included from get_global_id_3d.c:6:0:
    cl_simple.h:19:10: note: expected 'const size_t *' but argument is of type 'size_t (*)[3]'
    gcc -o get-global-id-3d get_global_id_3d.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    cc -g   -c -o mat_mul.o mat_mul.c
    gcc -o mat-mul mat_mul.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    cc -g   -c -o use_host_ptr.o use_host_ptr.c
    gcc -o use-host-ptr use_host_ptr.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    cc -g   -c -o copy_host_ptr.o copy_host_ptr.c
    gcc -o copy-host-ptr copy_host_ptr.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    cc -g   -c -o memset.o memset.c
    memset.c: In function 'main':
    memset.c:47:7: warning: format '%i' expects argument of type 'int', but argument 3 has type 'size_t' [-Wformat]
    gcc -o memset memset.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    cc -g   -c -o vec_load.o vec_load.c
    gcc -o vec-load vec_load.o cl_simple.o cl_util.o -L/usr/local/lib -lOpenCL
    Code:
    ./run_tests.sh
    Running ./math-int add 1 2 3
    Passed
    Running ./math-int add 2 1 3
    Passed
    Running ./math-int add -5 10 5
    Passed
    Running ./math-int add -1 -4 -5
    Passed
    Running ./math-int mul 4 5 20
    Passed
    Running ./math-int mul 8 0 0
    Passed
    Running ./math-int mul -3 8 -24
    Passed
    Running ./math-int mul -12 -6 72
    Passed
    Running ./math-int div 20 5 4
    Passed
    Running ./math-int div 23 5 4
    Passed
    Running ./math-int div 30 1 30
    Passed
    Running ./math-int div 57 -1 -57
    Passed
    Running ./math-int div 10 -2 -5
    Passed
    Running ./math-int div 17 -3 -5
    Passed
    Running ./math-int div -28 2 -14
    Passed
    Running ./math-int div -8 3 -2
    Passed
    Running ./math-int div -25 -5 5
    Passed
    Running ./math-int div -24 -5 4
    Passed
    Running ./math-int mod 18 6 0
    Passed
    Running ./math-int mod 59 12 11
    Passed
    Running ./math-int mod -20 5 0
    Passed
    Running ./math-int mod -18 5 -3
    Passed
    Running ./math-int mod 50 -10 0
    Passed
    Running ./math-int mod 16 -3 1
    Passed
    Running ./math-int mod 2147483647 12345 9172
    Passed
    Running ./math-int mod -2147483648 476 -128
    Passed
    Running ./math-int mod 10 20 10
    Passed
    Running ./math-int mod_nine 18 9 0
    Passed
    Running ./math-int mod_nine 23 9 5
    Passed
    Running ./math-int mod_four 20 4 0
    Passed
    Running ./math-int mod_four 5 4 1
    Passed
    Running ./get-global-id 100 100
    Passed
    Running ./get-global-id 250 1
    Passed
    Running ./math-int if_gt 5 4 1
    Passed
    Running ./math-int if_gt 5 6 0
    Passed
    Running ./math-int if_gt -20 10 0
    Passed
    Running ./math-int if_gt -5 8 0
    Passed
    Running ./math-int if_gt 12 -15 1
    Passed
    Running ./math-int if_gt 16 -3 1
    Passed
    Running ./math-int if_ge 8 7 1
    Passed
    Running ./math-int if_ge 10 10 1
    Passed
    Running ./math-int if_ge 20 30 0
    Passed
    Running ./math-int if_ge 3 -8 1
    Passed
    Running ./math-int if_ge -5 5 0
    Passed
    Running ./math-int if_ge -20 10 0
    Passed
    Running ./math-int if_eq 21 21 1
    Passed
    Running ./math-int if_eq 30 18 0
    Passed
    Running ./math-int if_eq -12 12 0
    Passed
    Running ./math-int if_eq 81 -81 0
    Passed
    Running ./math-int if_lt 2 10 1
    Passed
    Running ./math-int if_lt -20 3 1
    Passed
    Running ./math-int if_lt 15 3 0
    Passed
    Running ./math-int if_le 20 25 1
    Passed
    Running ./math-int if_le 18 18 1
    Passed
    Running ./math-int if_le -10 5 1
    Passed
    Running ./math-int if_le 18 9 0
    Passed
    Running ./math-int if_le 10 -20 0
    Passed
    Running ./math-int if_ne 10 9 1
    Passed
    Running ./math-int if_ne -20 20 1
    Passed
    Running ./math-int if_ne 31 -31 1
    Passed
    Running ./math-int if_ne 3 3 0
    Passed
    Running ./loop loop_lt 10
    Passed
    Running ./loop loop_le 10
    Passed
    Running ./loop loop_gt 10
    Passed
    Running ./loop loop_ge 10
    Passed
    Running ./math-int rotl 1 1 2
    Passed
    Running ./math-int rotl 1 32 1
    Passed
    Running ./math-int rotl -1 5 -1
    Passed
    Running ./math-int rotl 4096 23 8
    Passed
    Running ./use-host-ptr 10
    Passed
    Running ./vec-load
    Passed
    71 passes, 0 fails
    Code:
    ./hello_world
    There are 1 platforms.
    There are 1 GPU devices.
    clCreateContext() succeeded.
    clCreateCommandQueue() succeeded.
    clCreateProgramWithSource() suceeded.
    clBuildProgram() suceeded.
    clCreateKernel() suceeded.
    clCreateBuffer() succeeded.
    clSetKernelArg() succeeded.
    clEnqueueNDRangeKernel() suceeded.
    clFinish() succeeded.
    clEnqueueReadBuffer() suceeded.
    pi = 3.141590
    Thanks!!

    Jason

  3. #23
    Join Date
    May 2013
    Posts
    13

    Default

    Hi, I'm trying to replicate the opencl-example test on gentoo - I've got llvm, mesa, libclc, libdrm all built from the x11 overlay (running on 3.8.5 kernel), and the opencl-example seems to compile okay, but when I run it I get gpu lockups for each test (and if I was running X at the time, the whole machine becomes locked up).

    This is on A8-5600K (aruba) - is this chip supported at this time, or any other hints for what to look at?

  4. #24
    Join Date
    May 2011
    Posts
    33

    Default

    Quote Originally Posted by BradN View Post
    Hi, I'm trying to replicate the opencl-example test on gentoo - I've got llvm, mesa, libclc, libdrm all built from the x11 overlay (running on 3.8.5 kernel), and the opencl-example seems to compile okay, but when I run it I get gpu lockups for each test (and if I was running X at the time, the whole machine becomes locked up).

    This is on A8-5600K (aruba) - is this chip supported at this time, or any other hints for what to look at?
    Aruba is not very well supported yet. You need to disable virtual memory in mesa to avoid lockups. I'm hoping to look into this in the next few weeks.

Posting Permissions

  • You may not post new threads
  • You may not post replies
  • You may not post attachments
  • You may not edit your posts
  •