| 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
References:
Received: from culpepper.freedesktop.org (culpepper.freedesktop.org
[IPv6:2610:10:20:722:a800:ff:fe98:4b55])
by gabe.freedesktop.org (Postfix) with ESMTP id BE1356E12E
for ; Sat, 12 Aug 2017 07:48:04 +0000 (UTC)
In-Reply-To: ,
List-Archive:
List-Post:
List-Help:
List-Subscribe: ,
Errors-To: dri-devel-bounces@lists.freedesktop.org
Sender: "dri-devel"
To: dri-devel@lists.freedesktop.org
List-Id: dri-devel@lists.freedesktop.org
--===============1653823809==
Content-Type: multipart/alternative; boundary="15025240840.c1D45B2d.14838";
charset="UTF-8"
--15025240840.c1D45B2d.14838
Date: Sat, 12 Aug 2017 07:48:04 +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=3D102179
--- Comment #1 from Janpieter Sollie ---
Created attachment 133451
--> https://bugs.freedesktop.org/attachment.cgi?id=3D133451&action=3Dedit
gdb backtrace
--=20
You are receiving this mail because:
You are the assignee for the bug.=
--15025240840.c1D45B2d.14838
Date: Sat, 12 Aug 2017 07:48:04 +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
Commen=
t # 1
on bug 10217=
9
from Janpieter Sollie
Created attachment 133451
References:
Received: from culpepper.freedesktop.org (culpepper.freedesktop.org
[IPv6:2610:10:20:722:a800:ff:fe98:4b55])
by gabe.freedesktop.org (Postfix) with ESMTP id 4FDE76E1CC
for ; Sat, 12 Aug 2017 07:50:03 +0000 (UTC)
In-Reply-To: ,
List-Archive:
List-Post:
List-Help:
List-Subscribe: ,
Errors-To: dri-devel-bounces@lists.freedesktop.org
Sender: "dri-devel"
To: dri-devel@lists.freedesktop.org
List-Id: dri-devel@lists.freedesktop.org
--===============1076123594==
Content-Type: multipart/alternative; boundary="15025242030.ce8e35F9A.15891";
charset="UTF-8"
--15025242030.ce8e35F9A.15891
Date: Sat, 12 Aug 2017 07:50:03 +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=3D102179
--- Comment #2 from Janpieter Sollie ---
Created attachment 133452
--> https://bugs.freedesktop.org/attachment.cgi?id=3D133452&action=3Dedit
dmesg output reporting page fault
--=20
You are receiving this mail because:
You are the assignee for the bug.=
--15025242030.ce8e35F9A.15891
Date: Sat, 12 Aug 2017 07:50:03 +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
Commen=
t # 2
on bug 10217=
9
from Janpieter Sollie
Created attach=
ment 133452 [details]
dmesg output reporting page fault
You are receiving this mail because:
- You are the assignee for the bug.
=
--15025242030.ce8e35F9A.15891--
--===============1076123594==
Content-Type: text/plain; charset="utf-8"
MIME-Version: 1.0
Content-Transfer-Encoding: base64
Content-Disposition: inline
X19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX18KZHJpLWRldmVs
IG1haWxpbmcgbGlzdApkcmktZGV2ZWxAbGlzdHMuZnJlZWRlc2t0b3Aub3JnCmh0dHBzOi8vbGlz
dHMuZnJlZWRlc2t0b3Aub3JnL21haWxtYW4vbGlzdGluZm8vZHJpLWRldmVsCg==
--===============1076123594==--
From mboxrd@z Thu Jan 1 00:00:00 1970
From: bugzilla-daemon@freedesktop.org
Subject: [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT
Date: Sat, 12 Aug 2017 09:01:46 +0000
Message-ID:
Received: from culpepper.freedesktop.org (culpepper.freedesktop.org
[IPv6:2610:10:20:722:a800:ff:fe98:4b55])
by gabe.freedesktop.org (Postfix) with ESMTP id CA00B6E28B
for ; Sat, 12 Aug 2017 09:01:46 +0000 (UTC)
In-Reply-To: ,
List-Archive:
List-Post:
List-Help:
List-Subscribe: ,
Errors-To: dri-devel-bounces@lists.freedesktop.org
Sender: "dri-devel"
To: dri-devel@lists.freedesktop.org
List-Id: dri-devel@lists.freedesktop.org
--===============0043677070==
Content-Type: multipart/alternative; boundary="15025285060.6c1e6Ccf3.862";
charset="UTF-8"
--15025285060.6c1e6Ccf3.862
Date: Sat, 12 Aug 2017 09:01:46 +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=3D102179
Janpieter Sollie changed:
What |Removed |Added
----------------------------------------------------------------------------
See Also| |https://bugs.freedesktop.or
| |g/show_bug.cgi?id=3D100199
--=20
You are receiving this mail because:
You are the assignee for the bug.=
--15025285060.6c1e6Ccf3.862
Date: Sat, 12 Aug 2017 09:01:46 +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
What
Removed
Added
See Also
https://bugs.freedesktop.org/show_bug.cgi?id=3D100199
You are receiving this mail because:
- You are the assignee for the bug.
=
--15025285060.6c1e6Ccf3.862--
--===============0043677070==
Content-Type: text/plain; charset="utf-8"
MIME-Version: 1.0
Content-Transfer-Encoding: base64
Content-Disposition: inline
X19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX18KZHJpLWRldmVs
IG1haWxpbmcgbGlzdApkcmktZGV2ZWxAbGlzdHMuZnJlZWRlc2t0b3Aub3JnCmh0dHBzOi8vbGlz
dHMuZnJlZWRlc2t0b3Aub3JnL21haWxtYW4vbGlzdGluZm8vZHJpLWRldmVsCg==
--===============0043677070==--
From mboxrd@z Thu Jan 1 00:00:00 1970
From: bugzilla-daemon@freedesktop.org
Subject: [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT
Date: Sat, 12 Aug 2017 14:40:54 +0000
Message-ID:
Received: from culpepper.freedesktop.org (culpepper.freedesktop.org
[131.252.210.165])
by gabe.freedesktop.org (Postfix) with ESMTP id AA19089C51
for ; Sat, 12 Aug 2017 14:40:54 +0000 (UTC)
In-Reply-To: ,
List-Archive:
List-Post:
List-Help:
List-Subscribe: ,
Errors-To: dri-devel-bounces@lists.freedesktop.org
Sender: "dri-devel"
To: dri-devel@lists.freedesktop.org
List-Id: dri-devel@lists.freedesktop.org
--===============0984858901==
Content-Type: multipart/alternative; boundary="15025488540.6cCBA5.14177";
charset="UTF-8"
--15025488540.6cCBA5.14177
Date: Sat, 12 Aug 2017 14:40:54 +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=3D102179
Janpieter Sollie changed:
What |Removed |Added
----------------------------------------------------------------------------
Severity|normal |major
--- Comment #3 from Janpieter Sollie ---
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 b=
ack,
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)
--=20
You are receiving this mail because:
You are the assignee for the bug.=
--15025488540.6cCBA5.14177
Date: Sat, 12 Aug 2017 14:40:54 +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
What
Removed
Added
Severity
normal
major
Commen=
t # 3
on bug 10217=
9
from Janpieter Sollie
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 b=
ack,
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.
=
--15025488540.6cCBA5.14177--
--===============0984858901==
Content-Type: text/plain; charset="utf-8"
MIME-Version: 1.0
Content-Transfer-Encoding: base64
Content-Disposition: inline
X19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX18KZHJpLWRldmVs
IG1haWxpbmcgbGlzdApkcmktZGV2ZWxAbGlzdHMuZnJlZWRlc2t0b3Aub3JnCmh0dHBzOi8vbGlz
dHMuZnJlZWRlc2t0b3Aub3JnL21haWxtYW4vbGlzdGluZm8vZHJpLWRldmVsCg==
--===============0984858901==--
From mboxrd@z Thu Jan 1 00:00:00 1970
From: bugzilla-daemon@freedesktop.org
Subject: [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT
Date: Tue, 15 Aug 2017 13:40:13 +0000
Message-ID:
Received: from culpepper.freedesktop.org (culpepper.freedesktop.org
[131.252.210.165])
by gabe.freedesktop.org (Postfix) with ESMTP id 52D5F88005
for ; Tue, 15 Aug 2017 13:40:13 +0000 (UTC)
In-Reply-To: ,
List-Archive:
List-Post:
List-Help:
List-Subscribe: ,
Errors-To: dri-devel-bounces@lists.freedesktop.org
Sender: "dri-devel"
To: dri-devel@lists.freedesktop.org
List-Id: dri-devel@lists.freedesktop.org
--===============0049431886==
Content-Type: multipart/alternative; boundary="15028044130.1D30.7314";
charset="UTF-8"
--15028044130.1D30.7314
Date: Tue, 15 Aug 2017 13:40:13 +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=3D102179
Vedran Mileti=C4=87 changed:
What |Removed |Added
----------------------------------------------------------------------------
Blocks| |99553
Referenced Bugs:
https://bugs.freedesktop.org/show_bug.cgi?id=3D99553
[Bug 99553] Tracker bug for runnning OpenCL applications on Clover
--=20
You are receiving this mail because:
You are the assignee for the bug.=
--15028044130.1D30.7314
Date: Tue, 15 Aug 2017 13:40:13 +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
What
Removed
Added
Blocks
99553
Referenced Bugs:
You are receiving this mail because:
- You are the assignee for the bug.
=
--15028044130.1D30.7314--
--===============0049431886==
Content-Type: text/plain; charset="utf-8"
MIME-Version: 1.0
Content-Transfer-Encoding: base64
Content-Disposition: inline
X19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX18KZHJpLWRldmVs
IG1haWxpbmcgbGlzdApkcmktZGV2ZWxAbGlzdHMuZnJlZWRlc2t0b3Aub3JnCmh0dHBzOi8vbGlz
dHMuZnJlZWRlc2t0b3Aub3JnL21haWxtYW4vbGlzdGluZm8vZHJpLWRldmVsCg==
--===============0049431886==--
From mboxrd@z Thu Jan 1 00:00:00 1970
From: bugzilla-daemon@freedesktop.org
Subject: [Bug 102179] clEnqueueReadBuffer VM_PAGE FAULT
Date: Wed, 25 Sep 2019 17:59:44 +0000
Message-ID:
Received: from culpepper.freedesktop.org (culpepper.freedesktop.org
[131.252.210.165])
by gabe.freedesktop.org (Postfix) with ESMTP id 9E1BB6EC4D
for ; Wed, 25 Sep 2019 17:59:44 +0000 (UTC)
In-Reply-To: ,
List-Archive:
List-Post:
List-Help:
List-Subscribe: ,
Errors-To: dri-devel-bounces@lists.freedesktop.org
Sender: "dri-devel"
To: dri-devel@lists.freedesktop.org
List-Id: dri-devel@lists.freedesktop.org
--===============1674364071==
Content-Type: multipart/alternative; boundary="15694343842.BEEeA.32305"
Content-Transfer-Encoding: 7bit
--15694343842.BEEeA.32305
Date: Wed, 25 Sep 2019 17:59: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=3D102179
GitLab Migration User changed:
What |Removed |Added
----------------------------------------------------------------------------
Status|NEW |RESOLVED
Resolution|--- |MOVED
--- Comment #4 from GitLab Migration User ---
-- 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/127=
5.
--=20
You are receiving this mail because:
You are the assignee for the bug.=
--15694343842.BEEeA.32305
Date: Wed, 25 Sep 2019 17:59: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
What
Removed
Added
Status
NEW
RESOLVED
Resolution
---
MOVED
Commen=
t # 4
on bug 10217=
9
from GitLab Migration User
-- 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.
=
--15694343842.BEEeA.32305--
--===============1674364071==
Content-Type: text/plain; charset="utf-8"
MIME-Version: 1.0
Content-Transfer-Encoding: base64
Content-Disposition: inline
X19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX18KZHJpLWRldmVs
IG1haWxpbmcgbGlzdApkcmktZGV2ZWxAbGlzdHMuZnJlZWRlc2t0b3Aub3JnCmh0dHBzOi8vbGlz
dHMuZnJlZWRlc2t0b3Aub3JnL21haWxtYW4vbGlzdGluZm8vZHJpLWRldmVs
--===============1674364071==--