[Bug 99552] Make Advanced Simulation Library (ASL) OpenCL GPU support work on Clover and RadeonSI

[Bug 99552] Make Advanced Simulation Library (ASL) OpenCL GPU support work on Clover and RadeonSI

[bugzilla-daemon]

[-- Attachment #1.1: Type: text/plain, Size: 2010 bytes --]

https://bugs.freedesktop.org/show_bug.cgi?id=99552

            Bug ID: 99552
           Summary: Make Advanced Simulation Library (ASL) OpenCL GPU
                    support work on Clover and RadeonSI
           Product: Mesa
           Version: git
          Hardware: All
                OS: All
            Status: NEW
          Severity: normal
          Priority: medium
         Component: Drivers/Gallium/radeonsi
          Assignee: dri-devel@lists.freedesktop.org
          Reporter: vedran@miletic.net
        QA Contact: dri-devel@lists.freedesktop.org

Advanced Simulation Library (ASL) is a partial differential equation solver
that supports running with OpenCL. When using it on Mesa/radeonsi/LLVM/AMDGPU,
test/testACL/testKernel.cc [1] partially works but ultimately fails with:

$ ./testKernel
Test of "copy" function... Ok
Test of Kernel with double... Ok
Test of KernelSIMD... Ok
Test of KernelSIMDUA... Ok
Test of kernel with PrivateVariable... Ok
Test of kernel with PrivateArray...
                        BUILD LOG
 ************************************************
<unknown>:0:0: in function compute_4 void (i32 addrspace(1)*, float
addrspace(1)*): invalid addrspacecast

 ************************************************

                        KERNEL SOURCE CODE
 ------------------------------------------------
#pragma OPENCL EXTENSION cl_khr_fp64 : disable

__kernel void compute_4(__global int *a_i1,
                        __global float *a_f8)
{
        uint index = get_global_id(0);
        float pa_f1[6] = {-9, 2, 0, 15, 1, 3};
        (a_f8[index]=pa_f1[a_i1[index]]);
}
 ------------------------------------------------
terminate called after throwing an instance of 'std::logic_error'
  what():  ASL ERROR: Program::build() (-11).
Aborted (core dumped)

[1]
https://github.com/AvtechScientific/ASL/blob/master/test/testACL/testKernel.cc

-- 
You are receiving this mail because:
You are the assignee for the bug.

[-- Attachment #1.2: Type: text/html, Size: 3508 bytes --]

[-- Attachment #2: Type: text/plain, Size: 160 bytes --]

_______________________________________________
dri-devel mailing list
dri-devel@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/dri-devel

[Bug 99552] Make Advanced Simulation Library (ASL) OpenCL GPU support work on Clover and RadeonSI

[bugzilla-daemon]

[-- Attachment #1.1: Type: text/plain, Size: 513 bytes --]

https://bugs.freedesktop.org/show_bug.cgi?id=99552

Vedran Miletić <vedran@miletic.net> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
             Blocks|                            |99553


Referenced Bugs:

https://bugs.freedesktop.org/show_bug.cgi?id=99553
[Bug 99553] Tracker bug for runnning OpenCL applications on Clover
-- 
You are receiving this mail because:
You are the assignee for the bug.

[-- Attachment #1.2: Type: text/html, Size: 1610 bytes --]

[-- Attachment #2: Type: text/plain, Size: 160 bytes --]

_______________________________________________
dri-devel mailing list
dri-devel@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/dri-devel

[Bug 99552] Make Advanced Simulation Library (ASL) OpenCL GPU support work on Clover and RadeonSI

[bugzilla-daemon]

[-- Attachment #1.1: Type: text/plain, Size: 1915 bytes --]

https://bugs.freedesktop.org/show_bug.cgi?id=99552

--- Comment #1 from Vedran Miletić <vedran@miletic.net> ---
How to test:

$ mkdir build; cd build
$ cmake -DWITH_TESTS=ON ..
$ make -j
$ make test

Right now, Mesa/LLVM latest git pulled half an hour ago I get:

Running tests...
Test project /users/miletivn/workspace/ASL/build
      Start  1: testABDFormat
 1/10 Test  #1: testABDFormat ....................   Passed    0.07 sec
      Start  2: testVectorOfElements
 2/10 Test  #2: testVectorOfElements .............   Passed    5.27 sec
      Start  3: testMatrixOfElements
 3/10 Test  #3: testMatrixOfElements .............   Passed    7.89 sec
      Start  4: testKernel
 4/10 Test  #4: testKernel .......................***Exception: Other 13.94 sec
      Start  5: testOperators
 5/10 Test  #5: testOperators ....................   Passed    7.88 sec
      Start  6: testKernelMerger
 6/10 Test  #6: testKernelMerger .................   Passed    2.65 sec
      Start  7: testPrivateVar
 7/10 Test  #7: testPrivateVar ...................***Exception: Other  3.22 sec
      Start  8: testASLData
 8/10 Test  #8: testASLData ......................   Passed   13.72 sec
      Start  9: testDistanceFunction
 9/10 Test  #9: testDistanceFunction .............   Passed   42.43 sec
      Start 10: testReductionFunction
10/10 Test #10: testReductionFunction ............   Passed   29.24 sec

80% tests passed, 2 tests failed out of 10

Label Time Summary:
DoublePrecision    =  85.62 sec (3 tests)
Performance        =   3.22 sec (1 test)

Total Test time (real) = 126.34 sec

The following tests FAILED:
          4 - testKernel (OTHER_FAULT)
          7 - testPrivateVar (OTHER_FAULT)
Errors while running CTest
Makefile:61: recipe for target 'test' failed
make: *** [test] Error 8

-- 
You are receiving this mail because:
You are the assignee for the bug.

[-- Attachment #1.2: Type: text/html, Size: 2770 bytes --]

[-- Attachment #2: Type: text/plain, Size: 160 bytes --]

_______________________________________________
dri-devel mailing list
dri-devel@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/dri-devel

[Bug 99552] Make Advanced Simulation Library (ASL) OpenCL GPU support work on Clover and RadeonSI

[bugzilla-daemon]

[-- Attachment #1.1: Type: text/plain, Size: 479 bytes --]

https://bugs.freedesktop.org/show_bug.cgi?id=99552

--- Comment #2 from Vedran Miletić <vedran@miletic.net> ---
(In reply to Vedran Miletić from comment #1)
>       Start  7: testPrivateVar
>  7/10 Test  #7: testPrivateVar ...................***Exception: Other  3.22
> sec

Adding native_rsqrt fixes this, patch will appear here:
http://lists.llvm.org/pipermail/libclc-dev/2017-February/

-- 
You are receiving this mail because:
You are the assignee for the bug.

[-- Attachment #1.2: Type: text/html, Size: 1482 bytes --]

[-- Attachment #2: Type: text/plain, Size: 160 bytes --]

_______________________________________________
dri-devel mailing list
dri-devel@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/dri-devel

[Bug 99552] Make Advanced Simulation Library (ASL) OpenCL GPU support work on Clover and RadeonSI

[bugzilla-daemon]

[-- Attachment #1.1: Type: text/plain, Size: 567 bytes --]

https://bugs.freedesktop.org/show_bug.cgi?id=99552

Vedran Miletić <vedran@miletic.net> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
         Resolution|---                         |FIXED
             Status|NEW                         |RESOLVED

--- Comment #3 from Vedran Miletić <vedran@miletic.net> ---
Fixed https://reviews.llvm.org/D27283 https://reviews.llvm.org/rL294786

-- 
You are receiving this mail because:
You are the assignee for the bug.

[-- Attachment #1.2: Type: text/html, Size: 2269 bytes --]

[-- Attachment #2: Type: text/plain, Size: 160 bytes --]

_______________________________________________
dri-devel mailing list
dri-devel@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/dri-devel