From mboxrd@z Thu Jan 1 00:00:00 1970 From: bugzilla-daemon@freedesktop.org Subject: [Bug 99552] Make Advanced Simulation Library (ASL) OpenCL GPU support work on Clover and RadeonSI Date: Thu, 26 Jan 2017 19:33:23 +0000 Message-ID: Mime-Version: 1.0 Content-Type: multipart/mixed; boundary="===============1620488104==" Return-path: Received: from culpepper.freedesktop.org (culpepper.freedesktop.org [IPv6:2610:10:20:722:a800:ff:fe98:4b55]) by gabe.freedesktop.org (Postfix) with ESMTP id 60FD76E2B4 for ; Thu, 26 Jan 2017 19:33:23 +0000 (UTC) List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: dri-devel-bounces@lists.freedesktop.org Sender: "dri-devel" To: dri-devel@lists.freedesktop.org List-Id: dri-devel@lists.freedesktop.org --===============1620488104== Content-Type: multipart/alternative; boundary="14854592030.6bacD2.28386"; charset="UTF-8" --14854592030.6bacD2.28386 Date: Thu, 26 Jan 2017 19:33:23 +0000 MIME-Version: 1.0 Content-Type: text/plain; charset="UTF-8" Content-Transfer-Encoding: quoted-printable X-Bugzilla-URL: http://bugs.freedesktop.org/ Auto-Submitted: auto-generated https://bugs.freedesktop.org/show_bug.cgi?id=3D99552 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/AMDG= PU, 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 ************************************************ :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 =3D get_global_id(0); float pa_f1[6] =3D {-9, 2, 0, 15, 1, 3}; (a_f8[index]=3Dpa_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 --=20 You are receiving this mail because: You are the assignee for the bug.= --14854592030.6bacD2.28386 Date: Thu, 26 Jan 2017 19:33:23 +0000 MIME-Version: 1.0 Content-Type: text/html; charset="UTF-8" Content-Transfer-Encoding: quoted-printable X-Bugzilla-URL: http://bugs.freedesktop.org/ Auto-Submitted: auto-generated
Bug ID 99552
Summary Make Advanced Simulation Library (ASL) OpenCL GPU support wor= k 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 eq=
uation solver
that supports running with OpenCL. When using it on Mesa/radeonsi/LLVM/AMDG=
PU,
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 =3D get_global_id(0);
        float pa_f1[6] =3D {-9, 2, 0, 15, 1, 3};
        (a_f8[index]=3Dpa_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/te=
stACL/testKernel.cc


You are receiving this mail because:
  • You are the assignee for the bug.
= --14854592030.6bacD2.28386-- --===============1620488104== Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: base64 Content-Disposition: inline X19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX18KZHJpLWRldmVs IG1haWxpbmcgbGlzdApkcmktZGV2ZWxAbGlzdHMuZnJlZWRlc2t0b3Aub3JnCmh0dHBzOi8vbGlz dHMuZnJlZWRlc2t0b3Aub3JnL21haWxtYW4vbGlzdGluZm8vZHJpLWRldmVsCg== --===============1620488104==--