* [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT
@ 2017-08-12 7:46 bugzilla-daemon
2017-08-12 7:48 ` bugzilla-daemon
` (5 more replies)
0 siblings, 6 replies; 7+ messages in thread
From: bugzilla-daemon @ 2017-08-12 7:46 UTC (permalink / raw)
To: dri-devel
[-- Attachment #1.1: Type: text/plain, Size: 1216 bytes --]
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
--
You are receiving this mail because:
You are the assignee for the bug.
[-- Attachment #1.2: Type: text/html, Size: 2692 bytes --]
[-- Attachment #2: Type: text/plain, Size: 160 bytes --]
_______________________________________________
dri-devel mailing list
dri-devel@lists.freedesktop.org
https://lists.freedesktop.org/mailman/listinfo/dri-devel
^ permalink raw reply [flat|nested] 7+ messages in thread* [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT 2017-08-12 7:46 [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT bugzilla-daemon @ 2017-08-12 7:48 ` bugzilla-daemon 2017-08-12 7:50 ` bugzilla-daemon ` (4 subsequent siblings) 5 siblings, 0 replies; 7+ messages in thread From: bugzilla-daemon @ 2017-08-12 7:48 UTC (permalink / raw) To: dri-devel [-- Attachment #1.1: Type: text/plain, Size: 319 bytes --] 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 -- You are receiving this mail because: You are the assignee for the bug. [-- Attachment #1.2: Type: text/html, Size: 1199 bytes --] [-- Attachment #2: Type: text/plain, Size: 160 bytes --] _______________________________________________ dri-devel mailing list dri-devel@lists.freedesktop.org https://lists.freedesktop.org/mailman/listinfo/dri-devel ^ permalink raw reply [flat|nested] 7+ messages in thread
* [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT 2017-08-12 7:46 [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT bugzilla-daemon 2017-08-12 7:48 ` bugzilla-daemon @ 2017-08-12 7:50 ` bugzilla-daemon 2017-08-12 9:01 ` bugzilla-daemon ` (3 subsequent siblings) 5 siblings, 0 replies; 7+ messages in thread From: bugzilla-daemon @ 2017-08-12 7:50 UTC (permalink / raw) To: dri-devel [-- Attachment #1.1: Type: text/plain, Size: 339 bytes --] 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 -- You are receiving this mail because: You are the assignee for the bug. [-- Attachment #1.2: Type: text/html, Size: 1259 bytes --] [-- Attachment #2: Type: text/plain, Size: 160 bytes --] _______________________________________________ dri-devel mailing list dri-devel@lists.freedesktop.org https://lists.freedesktop.org/mailman/listinfo/dri-devel ^ permalink raw reply [flat|nested] 7+ messages in thread
* [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT 2017-08-12 7:46 [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT bugzilla-daemon 2017-08-12 7:48 ` bugzilla-daemon 2017-08-12 7:50 ` bugzilla-daemon @ 2017-08-12 9:01 ` bugzilla-daemon 2017-08-12 14:40 ` bugzilla-daemon ` (2 subsequent siblings) 5 siblings, 0 replies; 7+ messages in thread From: bugzilla-daemon @ 2017-08-12 9:01 UTC (permalink / raw) To: dri-devel [-- Attachment #1.1: Type: text/plain, Size: 478 bytes --] 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 -- You are receiving this mail because: You are the assignee for the bug. [-- Attachment #1.2: Type: text/html, Size: 1132 bytes --] [-- Attachment #2: Type: text/plain, Size: 160 bytes --] _______________________________________________ dri-devel mailing list dri-devel@lists.freedesktop.org https://lists.freedesktop.org/mailman/listinfo/dri-devel ^ permalink raw reply [flat|nested] 7+ messages in thread
* [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT 2017-08-12 7:46 [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT bugzilla-daemon ` (2 preceding siblings ...) 2017-08-12 9:01 ` bugzilla-daemon @ 2017-08-12 14:40 ` bugzilla-daemon 2017-08-15 13:40 ` bugzilla-daemon 2019-09-25 17:59 ` bugzilla-daemon 5 siblings, 0 replies; 7+ messages in thread From: bugzilla-daemon @ 2017-08-12 14:40 UTC (permalink / raw) To: dri-devel [-- Attachment #1.1: Type: text/plain, Size: 1575 bytes --] 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) -- You are receiving this mail because: You are the assignee for the bug. [-- Attachment #1.2: Type: text/html, Size: 2884 bytes --] [-- Attachment #2: Type: text/plain, Size: 160 bytes --] _______________________________________________ dri-devel mailing list dri-devel@lists.freedesktop.org https://lists.freedesktop.org/mailman/listinfo/dri-devel ^ permalink raw reply [flat|nested] 7+ messages in thread
* [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT 2017-08-12 7:46 [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT bugzilla-daemon ` (3 preceding siblings ...) 2017-08-12 14:40 ` bugzilla-daemon @ 2017-08-15 13:40 ` bugzilla-daemon 2019-09-25 17:59 ` bugzilla-daemon 5 siblings, 0 replies; 7+ messages in thread From: bugzilla-daemon @ 2017-08-15 13:40 UTC (permalink / raw) To: dri-devel [-- Attachment #1.1: Type: text/plain, Size: 514 bytes --] 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 -- You are receiving this mail because: You are the assignee for the bug. [-- Attachment #1.2: Type: text/html, Size: 1560 bytes --] [-- Attachment #2: Type: text/plain, Size: 160 bytes --] _______________________________________________ dri-devel mailing list dri-devel@lists.freedesktop.org https://lists.freedesktop.org/mailman/listinfo/dri-devel ^ permalink raw reply [flat|nested] 7+ messages in thread
* [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT 2017-08-12 7:46 [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT bugzilla-daemon ` (4 preceding siblings ...) 2017-08-15 13:40 ` bugzilla-daemon @ 2019-09-25 17:59 ` bugzilla-daemon 5 siblings, 0 replies; 7+ messages in thread From: bugzilla-daemon @ 2019-09-25 17:59 UTC (permalink / raw) To: dri-devel [-- Attachment #1.1: Type: text/plain, Size: 842 bytes --] 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. -- You are receiving this mail because: You are the assignee for the bug. [-- Attachment #1.2: Type: text/html, Size: 2397 bytes --] [-- Attachment #2: Type: text/plain, Size: 159 bytes --] _______________________________________________ dri-devel mailing list dri-devel@lists.freedesktop.org https://lists.freedesktop.org/mailman/listinfo/dri-devel ^ permalink raw reply [flat|nested] 7+ messages in thread
end of thread, other threads:[~2019-09-25 17:59 UTC | newest] Thread overview: 7+ messages (download: mbox.gz follow: Atom feed -- links below jump to the message on this page -- 2017-08-12 7:46 [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT bugzilla-daemon 2017-08-12 7:48 ` bugzilla-daemon 2017-08-12 7:50 ` bugzilla-daemon 2017-08-12 9:01 ` bugzilla-daemon 2017-08-12 14:40 ` bugzilla-daemon 2017-08-15 13:40 ` bugzilla-daemon 2019-09-25 17:59 ` bugzilla-daemon
This is a public inbox, see mirroring instructions for how to clone and mirror all data and code used for this inbox