Announcement

Collapse
No announcement yet.

AMD Radeon R600 GPU LLVM 3.3 Back-End Testing

Collapse
X
  • Filter
  • Time
  • Show
Clear All
new posts

  • #21
    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?

    Comment


    • #22
      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

      Comment


      • #23
        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?

        Comment


        • #24
          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.

          Comment

          Working...
          X