<html>
<head>
<base href="https://bugs.freedesktop.org/" />
</head>
<body><table border="1" cellspacing="0" cellpadding="8">
<tr>
<th>Bug ID</th>
<td><a class="bz_bug_link
bz_status_NEW "
title="NEW - drm_intel_gem_bo_context_exec() failed: Input/output error"
href="https://bugs.freedesktop.org/show_bug.cgi?id=93579">93579</a>
</td>
</tr>
<tr>
<th>Summary</th>
<td>drm_intel_gem_bo_context_exec() failed: Input/output error
</td>
</tr>
<tr>
<th>Product</th>
<td>DRI
</td>
</tr>
<tr>
<th>Version</th>
<td>unspecified
</td>
</tr>
<tr>
<th>Hardware</th>
<td>x86-64 (AMD64)
</td>
</tr>
<tr>
<th>OS</th>
<td>Linux (All)
</td>
</tr>
<tr>
<th>Status</th>
<td>NEW
</td>
</tr>
<tr>
<th>Severity</th>
<td>normal
</td>
</tr>
<tr>
<th>Priority</th>
<td>medium
</td>
</tr>
<tr>
<th>Component</th>
<td>DRM/Intel
</td>
</tr>
<tr>
<th>Assignee</th>
<td>intel-gfx-bugs@lists.freedesktop.org
</td>
</tr>
<tr>
<th>Reporter</th>
<td>frank.dittrich@mailbox.org
</td>
</tr>
<tr>
<th>QA Contact</th>
<td>intel-gfx-bugs@lists.freedesktop.org
</td>
</tr>
<tr>
<th>CC</th>
<td>intel-gfx-bugs@lists.freedesktop.org
</td>
</tr></table>
<p>
<div>
<pre>Created <span class=""><a href="attachment.cgi?id=120800" name="attach_120800" title="Contents of /sys/class/drm/card0/error">attachment 120800</a> <a href="attachment.cgi?id=120800&action=edit" title="Contents of /sys/class/drm/card0/error">[details]</a></span>
Contents of /sys/class/drm/card0/error
This is from dmesg:
[ 1791.185004] [drm] stuck on render ring
[ 1791.186261] [drm] GPU HANG: ecode 7:0:0x85ddfffc, in john [2277], reason:
Ring hung, action: reset
[ 1791.186265] [drm] GPU hangs can indicate a bug anywhere in the entire gfx
stack, including userspace.
[ 1791.186268] [drm] Please file a _new_ bug report on bugs.freedesktop.org
against DRI -> DRM/Intel
[ 1791.186270] [drm] drm/i915 developers can then reassign to the right
component if it's not a kernel issue.
[ 1791.186273] [drm] The gpu crash dump is required to analyze gpu hangs, so
please always attach it.
[ 1791.186275] [drm] GPU crash dump saved to /sys/class/drm/card0/error
[ 1791.188446] drm/i915: Resetting chip after gpu hang
[ 1797.181911] [drm] stuck on render ring
[ 1797.183147] [drm] GPU HANG: ecode 7:0:0x85ddfffc, in john [2277], reason:
Ring hung, action: reset
[ 1797.185338] drm/i915: Resetting chip after gpu hang
I am attaching the contents of /sys/class/drm/card0/error.
I got the error on a Fedora 22 system with kernel
4.4.0-0.rc6.git1.1.vanilla.knurd.1.fc22.x86_64.
The CPU is Intel(R) Core(TM) i5-4570 CPU @ 3.20GHz.
I built and installed beignet from latest master commit.
(master)beignet $ git describe --tags
Release_v1.0.0-654-gf749808
Then I built John the Ripper using a recent bleeding-jumbo commit
<a href="https://github.com/magnumripper/JohnTheRipper/commit/ca11872eaf094b0dbe90ba3f74fae5366d2b3125">https://github.com/magnumripper/JohnTheRipper/commit/ca11872eaf094b0dbe90ba3f74fae5366d2b3125</a>
(bleeding-jumbo)run $ git describe --tags
1.8.0.6-jumbo-1-1814-gca11872
(bleeding-jumbo)run $ ./john --list=build-info
Version: 1.8.0.6-jumbo-1-1814-gca11872
Build: linux-gnu 64-bit AVX2-ac OMP
SIMD: AVX2, interleaving: MD4:3 MD5:3 SHA1:1 SHA256:1 SHA512:1
$JOHN is ./
Format interface version: 13
Max. number of reported tunable costs: 3
Rec file version: REC4
Charset file version: CHR3
CHARSET_MIN: 1 (0x01)
CHARSET_MAX: 255 (0xff)
CHARSET_LENGTH: 24
SALT_HASH_SIZE: 1048576
Max. Markov mode level: 400
Max. Markov mode password length: 30
gcc version: 5.3.1
GNU libc version: 2.21 (loaded: 2.21)
OpenCL headers version: 1.2
Crypto library: OpenSSL
OpenSSL library version: 0100010bf
OpenSSL 1.0.1k-fips 8 Jan 2015
GMP library version: 6.0.0
Regex library version: 1.3 (loaded: 1.3.1)
File locking: fcntl()
fseek(): fseek
ftell(): ftell
fopen(): fopen
memmem(): System's
I got the GPU hang when running the self test for office2013-opencl format.
(bleeding-jumbo)run $ ./john --test=0 --format=office2013-opencl
Will run 4 OpenMP threads
Device 0: Intel(R) HD Graphics Haswell GT2 Desktop
Testing: office2013-opencl, MS Office 2013 (100,000 iterations) [SHA512 OpenCL
2x AES]... (4xOMP) Options used: -I ./kernels -cl-mad-enable -D__GPU__
-DDEVICE_INFO=34 -DSIZEOF_SIZE_T=8 -DDEV_VER_MAJOR=1 -DDEV_VER_MINOR=2
-D_OPENCL_COMPILER -DHASH_LOOPS=100 -DUNICODE_LENGTH=96 -DV_WIDTH=2
$JOHN/kernels/office2013_kernel.cl
Local worksize (LWS) 7, global worksize (GWS) 49
drm_intel_gem_bo_context_exec() failed: Input/output error
OpenCL CL_OUT_OF_RESOURCES error in opencl_office2013_fmt_plug.c:323 - failed
in clEnqueueNDRangeKernel
(bleeding-jumbo)run $ echo $?
1
I got similar problems with some older Linux kernels, beignet versions or John
the Ripper versions.
I have no idea what causes the GPU hang, but I doubt John the Ripper is to
blame.
John the Ripper's OpenCL formats work on various other GPUs.
Once I even tried that test after
# echo -n 0 > /sys/module/i915/parameters/enable_hangcheck
I had to switch off power after about half an hour.
Please let me know what else to test.
I would like to know what causes the GPU hang and how to fix or work around it.</pre>
</div>
</p>
<hr>
<span>You are receiving this mail because:</span>
<ul>
<li>You are the QA Contact for the bug.</li>
<li>You are on the CC list for the bug.</li>
<li>You are the assignee for the bug.</li>
</ul>
</body>
</html>