Bug 99540 - Make CP2K OpenCL GPU support work on Clover and RadeonSI (requires parts of OpenCL 1.2)
Summary: Make CP2K OpenCL GPU support work on Clover and RadeonSI (requires parts of O...
Alias: None
Product: Mesa
Classification: Unclassified
Component: Gallium/StateTracker/Clover (show other bugs)
Version: git
Hardware: Other All
: medium normal
Assignee: Vedran Miletić
QA Contact: Vedran Miletić
Depends on:
Blocks: 99553
  Show dependency treegraph
Reported: 2017-01-25 19:38 UTC by Vedran Miletić
Modified: 2019-09-18 17:55 UTC (History)
0 users

See Also:
i915 platform:
i915 features:


Description Vedran Miletić 2017-01-25 19:38:44 UTC
CP2K is a popular quantum chemistry software that provides limited/prototype support for GPU acceleration using OpenCL, but would be interested in expanding 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=466 @@@@@@@@@
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

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

 ===== Routine Calling Stack =====

            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
Comment 1 GitLab Migration User 2019-09-18 17:55:59 UTC
-- GitLab Migration Automatic Message --

This bug has been migrated to freedesktop.org's GitLab instance and has been closed from further activity.

You can subscribe and participate further through the new bug through this link to our GitLab instance: https://gitlab.freedesktop.org/mesa/mesa/issues/134.

Use of freedesktop.org services, including Bugzilla, is subject to our Code of Conduct. How we collect and use information is described in our Privacy Policy.