<html>
<head>
<base href="https://bugs.freedesktop.org/" />
</head>
<body>
<p>
<div>
<b><a class="bz_bug_link
bz_status_NEW "
title="NEW - OpenCL hangs with big kernels"
href="https://bugs.freedesktop.org/show_bug.cgi?id=70779#c5">Comment # 5</a>
on <a class="bz_bug_link
bz_status_NEW "
title="NEW - OpenCL hangs with big kernels"
href="https://bugs.freedesktop.org/show_bug.cgi?id=70779">bug 70779</a>
from <span class="vcard"><a class="email" href="mailto:EoD@xmw.de" title="EoD <EoD@xmw.de>"> <span class="fn">EoD</span></a>
</span></b>
<pre>Created <span class=""><a href="attachment.cgi?id=121742" name="attach_121742" title="dmesg after running the uint_add16() kernel">attachment 121742</a> <a href="attachment.cgi?id=121742&action=edit" title="dmesg after running the uint_add16() kernel">[details]</a></span>
dmesg after running the uint_add16() kernel
(In reply to Hristo Venev from <a href="show_bug.cgi?id=70779#c4">comment #4</a>)
<span class="quote">> Here are two kernels that fail:
> __kernel void uint_div(__global const uint *a, __global const uint *b,
> __global uint *c){
> c[0]=a[0]/b[0];
> }
> __kernel void uint_add16(__global const uint *a, __global const uint *b,
> __global uint *c){
> for(uint i=0;i<16;i++) c[i]=a[i]+b[i];
> }</span >
I actually can confirm that the 2nd kernel does cause a GPU stall in the radeon
driver (r600/Barts). It causes no problem with amdgpu (radeonsi/Tonga).
I am using kernel 4.5.0-rc3, current llvm 3.8 branch and current mesa git.
As I am not overly good with OpenCL, is this kernel somehow problematic?</pre>
</div>
</p>
<hr>
<span>You are receiving this mail because:</span>
<ul>
<li>You are the assignee for the bug.</li>
</ul>
</body>
</html>