Page 1 of 2 12 LastLast
Results 1 to 10 of 22

Thread: AMD Evergreen Compute Support Lands Mainline

Hybrid View

  1. #1
    Join Date
    Jan 2007
    Posts
    15,640

    Default AMD Evergreen Compute Support Lands Mainline

    Phoronix: AMD Evergreen Compute Support Lands Mainline

    There were more OpenCL/compute-related commits to Mesa Git master on Friday afternoon. The main item is that the Radeon HD 5000 series has its compute support hooked-up...

    http://www.phoronix.com/vr.php?view=MTExMTk

  2. #2
    Join Date
    Jun 2010
    Location
    ฿ 16LDJ6Hrd1oN3nCoFL7BypHSEYL84ca1JR
    Posts
    1,052

    Default

    For everybody who wants to go to libclc without going through one additional phoronix page and one mailing list page:
    http://libclc.llvm.org/

    Not to confuse with libclc:
    http://libclc.sourceforge.net/

    Please, somebody rename one of those projects.


    So my real question: How do I build libclc? There's an awful lack of documentation on that page
    Code:
     /tmp/libclc (git)-[master] % for i in **/*.py; do sed -i 's#/usr/bin/python#/usr/bin/python2#g' "$i"; done
     /tmp/libclc (git)-[master] % ./configure.py --prefix=~/libclc
     /tmp/libclc (git)-[master] % make
    LLVM-CC nvptx--nvidiacl/lib/convert.cl.bc
    error: unknown target triple 'nvptx--nvidiacl', please use -triple or -arch
    make: *** [nvptx--nvidiacl/lib/convert.cl.bc] Error 1
     /tmp/libclc (git)-[master] %
    Is my llvm lacking PTX support?

  3. #3
    Join Date
    Jan 2009
    Posts
    1,765

    Default

    nice work devs


    benchmarks please

  4. #4
    Join Date
    May 2011
    Posts
    37

    Default

    Quote Originally Posted by ChrisXY View Post
    For everybody who wants to go to libclc without going through one additional phoronix page and one mailing list page:
    http://libclc.llvm.org/

    Not to confuse with libclc:
    http://libclc.sourceforge.net/

    Please, somebody rename one of those projects.


    So my real question: How do I build libclc? There's an awful lack of documentation on that page
    Code:
     /tmp/libclc (git)-[master] % for i in **/*.py; do sed -i 's#/usr/bin/python#/usr/bin/python2#g' "$i"; done
     /tmp/libclc (git)-[master] % ./configure.py --prefix=~/libclc
     /tmp/libclc (git)-[master] % make
    LLVM-CC nvptx--nvidiacl/lib/convert.cl.bc
    error: unknown target triple 'nvptx--nvidiacl', please use -triple or -arch
    make: *** [nvptx--nvidiacl/lib/convert.cl.bc] Error 1
     /tmp/libclc (git)-[master] %
    Is my llvm lacking PTX support?
    You need the current SVN version of LLVM to build the libclc from trunk. However, if you want to test out clover on r600g, you'll need to fetch my patched version of libclc here: http://cgit.freedesktop.org/~tstellar/libclc

    Full instructions for getting clover going on r600g can be found here: http://dri.freedesktop.org/wiki/GalliumCompute

  5. #5
    Join Date
    Jun 2010
    Location
    ฿ 16LDJ6Hrd1oN3nCoFL7BypHSEYL84ca1JR
    Posts
    1,052

    Default

    Quote Originally Posted by tstellar View Post
    Full instructions for getting clover going on r600g can be found here: http://dri.freedesktop.org/wiki/GalliumCompute
    If I need to patch llvm, then it too much for me right now. The article just made it sound so easy. ^That link should have been in the article...

    And by the way: keep up the good work.

  6. #6
    Join Date
    Dec 2011
    Posts
    2,194

    Default Great news

    Great news for all Evergreen owners.
    Watch out, maybe soon AMD drop support for the Evergreen too.
    They just dropped 2000, 3000, and 4000 series support. You're guys next.

  7. #7
    Join Date
    Sep 2008
    Posts
    989

    Default

    Congrats on this. Hopefully NI and SI support won't be too far behind (but in reality they probably will be, at least for SI).

    This came about 3 months too late for me. My HD5970 is no longer in my immediate possession.

  8. #8
    Join Date
    Feb 2011
    Location
    Ukraine
    Posts
    153

    Default

    Quote Originally Posted by tstellar View Post
    Full instructions for getting clover going on r600g can be found here: http://dri.freedesktop.org/wiki/GalliumCompute
    I build all with this instruction, but all opencl-examples shows me
    Code:
     /home/downloads/git/opencl-example/hello_world 
    radeon: Failed to get PCI ID, error number -13
    There are 1 platforms.
    clGetDeviceIDs() failed: CL_DEVICE_NOT_FOUND
    I use hd6770 (juniper).
    In what may be the problem?

    libclc has same warnings at build time
    Code:
    LINK utils/prepare-builtins
    LLVM-CC r600--/lib/workitem/get_global_id
    LLVM-CC r600--/lib/workitem/get_global_size.cl.bc
    LLVM-CC r600--/lib/convert.cl.bc
    ./generic/lib/convert.cl:69:19: warning: shift count >= width of type [-Wshift-count-overflow]
      return l > ((1UL<<32)-1) ? ((1UL<<32)-1) : l;
                      ^ ~~
    ./generic/lib/convert.cl:69:35: warning: shift count >= width of type [-Wshift-count-overflow]
      return l > ((1UL<<32)-1) ? ((1UL<<32)-1) : l;
                                      ^ ~~
    2 warnings generated.
    LLVM-CC r600--/lib/geometric/cross.cl.bc
    LLVM-CC r600--/lib/geometric/dot.cl.bc
    LLVM-CC r600--/lib/geometric/length.cl.bc

  9. #9
    Join Date
    May 2011
    Posts
    37

    Default

    Quote Originally Posted by Pontostroy View Post
    I build all with this instruction, but all opencl-examples shows me
    Code:
     /home/downloads/git/opencl-example/hello_world 
    radeon: Failed to get PCI ID, error number -13
    There are 1 platforms.
    clGetDeviceIDs() failed: CL_DEVICE_NOT_FOUND
    I use hd6770 (juniper).
    In what may be the problem?
    You need to run those programs as root if X is running.

    Quote Originally Posted by Pontostroy View Post
    libclc has same warnings at build time
    Code:
    LINK utils/prepare-builtins
    LLVM-CC r600--/lib/workitem/get_global_id
    LLVM-CC r600--/lib/workitem/get_global_size.cl.bc
    LLVM-CC r600--/lib/convert.cl.bc
    ./generic/lib/convert.cl:69:19: warning: shift count >= width of type [-Wshift-count-overflow]
      return l > ((1UL<<32)-1) ? ((1UL<<32)-1) : l;
                      ^ ~~
    ./generic/lib/convert.cl:69:35: warning: shift count >= width of type [-Wshift-count-overflow]
      return l > ((1UL<<32)-1) ? ((1UL<<32)-1) : l;
                                      ^ ~~
    2 warnings generated.
    LLVM-CC r600--/lib/geometric/cross.cl.bc
    LLVM-CC r600--/lib/geometric/dot.cl.bc
    LLVM-CC r600--/lib/geometric/length.cl.bc
    These warning shouldn't affect anything.

  10. #10
    Join Date
    Feb 2011
    Location
    Ukraine
    Posts
    153

    Default

    Quote Originally Posted by tstellar View Post
    You need to run those programs as root if X is running.
    .
    It works (almost).
    Code:
    /home/downloads/git/opencl-example/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.
    radeon: The kernel rejected CS, see dmesg for more information.
    clEnqueueNDRangeKernel() suceeded.
    clEnqueueReadBuffer() suceeded.
    pi = 0.000000
    Code:
    [  424.341250] radeon 0000:01:00.0: evergreen_surface_check_linear_aligned:209 cb pitch 8 invalid must be aligned with 128
    [  424.341254] radeon 0000:01:00.0: evergreen_cs_track_validate_cb:422 cb[0] invalid (0x00000000 0x00000000 0x00000010 0x04000134)
    [  424.341257] radeon 0000:01:00.0: evergreen_packet3_check:2110 invalid cmd stream 628
    [  424.341259] [drm:radeon_cs_ib_chunk] *ERROR* Invalid command stream !

Posting Permissions

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