Bug 99540

Summary: Make CP2K OpenCL GPU support work on Clover and RadeonSI (requires parts of OpenCL 1.2)
Product: Mesa Reporter: Vedran Miletić <vedran>
Component: Gallium/StateTracker/CloverAssignee: Vedran Miletić <vedran>
Status: RESOLVED MOVED QA Contact: Vedran Miletić <vedran>
Severity: normal    
Priority: medium    
Version: git   
Hardware: Other   
OS: All   
Whiteboard:
i915 platform: i915 features:
Bug Depends on:    
Bug Blocks: 99553    

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.