https://bugs.freedesktop.org/show_bug.cgi?id=102179
Bug ID: 102179 Summary: clEnqueueReadBuffer VM_PAGE FAULT Product: Mesa Version: 17.2 Hardware: x86-64 (AMD64) OS: Linux (All) Status: NEW Severity: normal Priority: medium Component: Drivers/Gallium/radeonsi Assignee: dri-devel@lists.freedesktop.org Reporter: janpieter.sollie@dommel.be QA Contact: dri-devel@lists.freedesktop.org
Created attachment 133450 --> https://bugs.freedesktop.org/attachment.cgi?id=133450&action=edit clinfo output
I'm not sure whether this is a mesa bug, so if it's not: I'm sorry Anyway, the problem: I have 2 GCN cards in my system, a 7700 and a R9 nano I'm using both with amdgpu on linux-4.13.0-r4 clinfo attached. My program causes a GPU fault on the 7700 when reading from a buffer. dmesg part attached this problem does not occur on the CPU or the R9 nano card GDB backtrace of thread calling the clEnqueueReadBuffer attached
If this is a known bug, or not yours, I'm sorry
https://bugs.freedesktop.org/show_bug.cgi?id=102179
--- Comment #1 from Janpieter Sollie janpieter.sollie@dommel.be --- Created attachment 133451 --> https://bugs.freedesktop.org/attachment.cgi?id=133451&action=edit gdb backtrace
https://bugs.freedesktop.org/show_bug.cgi?id=102179
--- Comment #2 from Janpieter Sollie janpieter.sollie@dommel.be --- Created attachment 133452 --> https://bugs.freedesktop.org/attachment.cgi?id=133452&action=edit dmesg output reporting page fault
https://bugs.freedesktop.org/show_bug.cgi?id=102179
Janpieter Sollie janpieter.sollie@dommel.be changed:
What |Removed |Added ---------------------------------------------------------------------------- See Also| |https://bugs.freedesktop.or | |g/show_bug.cgi?id=100199
https://bugs.freedesktop.org/show_bug.cgi?id=102179
Janpieter Sollie janpieter.sollie@dommel.be changed:
What |Removed |Added ---------------------------------------------------------------------------- Severity|normal |major
--- Comment #3 from Janpieter Sollie janpieter.sollie@dommel.be --- interesting note: the following code allows me to execute the clEnqueueReadBuffer: //set kernel arguments, limited to 1 clSetKernelArg ( devdb[nr_of_devices].kernel, 0, sizeof(devdb[nr_of_devices].output), &devdb[nr_of_devices].output);
//run kernel clEnqueueNDRangeKernel(..) //read buffer clEnqueueReadBuffer (((device*)device_obj)->command_queue, ((device*)device_obj)->output, CL_FALSE, 0, 16, ((device*)device_obj)->host_output, 0, NULL, NULL);
while it does not work with any 2nd, 3rd, ... kernel parameter, eg: clSetKernelArg ( devdb[nr_of_devices].kernel, 0, sizeof(devdb[nr_of_devices].output), &devdb[nr_of_devices].output); clSetKernelArg ( devdb[nr_of_devices].kernel, 1, sizeof(devdb[nr_of_devices].output2), &devdb[nr_of_devices].output2);
hangs at reading output. but no warning of VM_PAGE_FAULTS, these occur when output is the last argument
because I think this is a blocker for most OpenCL users to get their data back, I'm increasing it to major (also, this cannot be analyzed easily: every time the call hangs, I have to reboot my pc, as the process becomes a zombie)
https://bugs.freedesktop.org/show_bug.cgi?id=102179
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
https://bugs.freedesktop.org/show_bug.cgi?id=102179
GitLab Migration User gitlab-migration@fdo.invalid changed:
What |Removed |Added ---------------------------------------------------------------------------- Status|NEW |RESOLVED Resolution|--- |MOVED
--- Comment #4 from GitLab Migration User gitlab-migration@fdo.invalid --- -- 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/1275.
dri-devel@lists.freedesktop.org