From mboxrd@z Thu Jan  1 00:00:00 1970
From: bugzilla-daemon@freedesktop.org
Subject: [Bug 99540] Make CP2K OpenCL GPU support work on Clover and RadeonSI
 (requires parts of OpenCL 1.2)
Date: Wed, 25 Jan 2017 19:38:44 +0000
Message-ID: <bug-99540-502@http.bugs.freedesktop.org/>
Mime-Version: 1.0
Content-Type: multipart/mixed; boundary="===============1332326550=="
Return-path: <dri-devel-bounces@lists.freedesktop.org>
Received: from culpepper.freedesktop.org (culpepper.freedesktop.org
 [131.252.210.165])
 by gabe.freedesktop.org (Postfix) with ESMTP id C5BBD6EA67
 for <dri-devel@lists.freedesktop.org>; Wed, 25 Jan 2017 19:38:44 +0000 (UTC)
List-Unsubscribe: <https://lists.freedesktop.org/mailman/options/dri-devel>,
 <mailto:dri-devel-request@lists.freedesktop.org?subject=unsubscribe>
List-Archive: <https://lists.freedesktop.org/archives/dri-devel>
List-Post: <mailto:dri-devel@lists.freedesktop.org>
List-Help: <mailto:dri-devel-request@lists.freedesktop.org?subject=help>
List-Subscribe: <https://lists.freedesktop.org/mailman/listinfo/dri-devel>,
 <mailto:dri-devel-request@lists.freedesktop.org?subject=subscribe>
Errors-To: dri-devel-bounces@lists.freedesktop.org
Sender: "dri-devel" <dri-devel-bounces@lists.freedesktop.org>
To: dri-devel@lists.freedesktop.org
List-Id: dri-devel@lists.freedesktop.org


--===============1332326550==
Content-Type: multipart/alternative; boundary="14853731240.ff3A.14529";
 charset="UTF-8"


--14853731240.ff3A.14529
Date: Wed, 25 Jan 2017 19:38:44 +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=3D99540

            Bug ID: 99540
           Summary: Make CP2K OpenCL GPU support work on Clover and
                    RadeonSI (requires parts of OpenCL 1.2)
           Product: Mesa
           Version: git
          Hardware: Other
                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

CP2K is a popular quantum chemistry software that provides limited/prototype
support for GPU acceleration using OpenCL, but would be interested in expan=
ding
if there are users interested in using it: https://www.cp2k.org/dev:todo

Running CP2K with OpenCL results in:

input.cl:54:12: error: call to 'atom_cmpxchg' is ambiguous
/usr/local/include/clc/cl_khr_global_int32_base_atomics/atom_cmpxchg.h:1:29:
note: candidate function
/usr/local/include/clc/cl_khr_global_int32_base_atomics/atom_cmpxchg.h:2:38:
note: candidate function
/usr/local/include/clc/cl_khr_local_int32_base_atomics/atom_cmpxchg.h:1:29:
note: candidate function
/usr/local/include/clc/cl_khr_local_int32_base_atomics/atom_cmpxchg.h:2:38:
note: candidate function
@@@@@@@@@ END BUILD-DATA, SIZE=3D466 @@@@@@@@@
Error in: clCreateKernel -46
Error in: clSetKernelArg(0) -48
Error in: clSetKernelArg(1) -48
Error in: clSetKernelArg(2) -48
Error in: clSetKernelArg(3) -48
Error in: clEnqueueNDRangeKernel -48
CL user error: clEnqueueFillBuffer() requires OpenCL version 1.2 or greater.
9835 OPENCL RT Error line: 552, ERROR_CODE: -30


***************************************************************************=
****
 *   ___=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 *  /   \=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 * [ABORT]=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 *  \___/                       acc_devmem_setzero: failed=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 *    |=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 *  O/|=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 * /| |=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 * / \                                                    acc/acc_devmem.F:=
423
*

***************************************************************************=
****


 =3D=3D=3D=3D=3D Routine Calling Stack =3D=3D=3D=3D=3D

            8 dbcsr_mm_accdrv_process
            7 cannon_multiply_low_multrec
            6 cannon_multiply_low
            5 dbcsr_mm_cannon_multiply
            4 test_multiplies_multiproc
            3 dbcsr_run_tests
            2 lib_test
            1 CP2K

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

--14853731240.ff3A.14529
Date: Wed, 25 Jan 2017 19:38:44 +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

<html>
    <head>
      <base href=3D"https://bugs.freedesktop.org/">
    </head>
    <body><table border=3D"1" cellspacing=3D"0" cellpadding=3D"8">
        <tr>
          <th>Bug ID</th>
          <td><a class=3D"bz_bug_link=20
          bz_status_NEW "
   title=3D"NEW - Make CP2K OpenCL GPU support work on Clover and RadeonSI =
(requires parts of OpenCL 1.2)"
   href=3D"https://bugs.freedesktop.org/show_bug.cgi?id=3D99540">99540</a>
          </td>
        </tr>

        <tr>
          <th>Summary</th>
          <td>Make CP2K OpenCL GPU support work on Clover and RadeonSI (req=
uires parts of OpenCL 1.2)
          </td>
        </tr>

        <tr>
          <th>Product</th>
          <td>Mesa
          </td>
        </tr>

        <tr>
          <th>Version</th>
          <td>git
          </td>
        </tr>

        <tr>
          <th>Hardware</th>
          <td>Other
          </td>
        </tr>

        <tr>
          <th>OS</th>
          <td>All
          </td>
        </tr>

        <tr>
          <th>Status</th>
          <td>NEW
          </td>
        </tr>

        <tr>
          <th>Severity</th>
          <td>normal
          </td>
        </tr>

        <tr>
          <th>Priority</th>
          <td>medium
          </td>
        </tr>

        <tr>
          <th>Component</th>
          <td>Drivers/Gallium/radeonsi
          </td>
        </tr>

        <tr>
          <th>Assignee</th>
          <td>dri-devel&#64;lists.freedesktop.org
          </td>
        </tr>

        <tr>
          <th>Reporter</th>
          <td>vedran&#64;miletic.net
          </td>
        </tr>

        <tr>
          <th>QA Contact</th>
          <td>dri-devel&#64;lists.freedesktop.org
          </td>
        </tr></table>
      <p>
        <div>
        <pre>CP2K is a popular quantum chemistry software that provides lim=
ited/prototype
support for GPU acceleration using OpenCL, but would be interested in expan=
ding
if there are users interested in using it: <a href=3D"https://www.cp2k.org/=
dev:todo">https://www.cp2k.org/dev:todo</a>

Running CP2K with OpenCL results in:

input.cl:54:12: error: call to 'atom_cmpxchg' is ambiguous
/usr/local/include/clc/cl_khr_global_int32_base_atomics/atom_cmpxchg.h:1:29:
note: candidate function
/usr/local/include/clc/cl_khr_global_int32_base_atomics/atom_cmpxchg.h:2:38:
note: candidate function
/usr/local/include/clc/cl_khr_local_int32_base_atomics/atom_cmpxchg.h:1:29:
note: candidate function
/usr/local/include/clc/cl_khr_local_int32_base_atomics/atom_cmpxchg.h:2:38:
note: candidate function
&#64;&#64;&#64;&#64;&#64;&#64;&#64;&#64;&#64; END BUILD-DATA, SIZE=3D466 &#=
64;&#64;&#64;&#64;&#64;&#64;&#64;&#64;&#64;
Error in: clCreateKernel -46
Error in: clSetKernelArg(0) -48
Error in: clSetKernelArg(1) -48
Error in: clSetKernelArg(2) -48
Error in: clSetKernelArg(3) -48
Error in: clEnqueueNDRangeKernel -48
CL user error: clEnqueueFillBuffer() requires OpenCL version 1.2 or greater.
9835 OPENCL RT Error line: 552, ERROR_CODE: -30


***************************************************************************=
****
 *   ___=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 *  /   \=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 * [ABORT]=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 *  \___/                       acc_devmem_setzero: failed=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 *    |=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 *  O/|=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 * /| |=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=
=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20=20
*
 * / \                                                    acc/acc_devmem.F:=
423
*

***************************************************************************=
****


 =3D=3D=3D=3D=3D Routine Calling Stack =3D=3D=3D=3D=3D

            8 dbcsr_mm_accdrv_process
            7 cannon_multiply_low_multrec
            6 cannon_multiply_low
            5 dbcsr_mm_cannon_multiply
            4 test_multiplies_multiproc
            3 dbcsr_run_tests
            2 lib_test
            1 CP2K</pre>
        </div>
      </p>


      <hr>
      <span>You are receiving this mail because:</span>

      <ul>
          <li>You are the assignee for the bug.</li>
      </ul>
    </body>
</html>=

--14853731240.ff3A.14529--

--===============1332326550==
Content-Type: text/plain; charset="utf-8"
MIME-Version: 1.0
Content-Transfer-Encoding: base64
Content-Disposition: inline

X19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX18KZHJpLWRldmVs
IG1haWxpbmcgbGlzdApkcmktZGV2ZWxAbGlzdHMuZnJlZWRlc2t0b3Aub3JnCmh0dHBzOi8vbGlz
dHMuZnJlZWRlc2t0b3Aub3JnL21haWxtYW4vbGlzdGluZm8vZHJpLWRldmVsCg==

--===============1332326550==--