[Beignet] Program compilation crash on Ivy Bridge

[Nicolas Bourdaud]

Hi!

In beignet 0.9.3, beignet aborts in the middle on compilation with
compiling for ivybridge microarchitecture, while it compiles and runs
fine on Haswell.

I have provided a test program (test.cl) that shows the problem and the
generate log on haswell (haswell.log) and ivybridge (ivybridge.log). I
have tested on different ivybridge CPU  (HD4000, HD2500) and the issue
is the same. I have also tested on different haswell CPU (only HD4600)
and it always goes fine.

For information beignet has been tested for:
 - ivybridge using linux 3.14 compiled with llvm 3.4.
 - haswell using linux 3.14 compiled with llvm 3.4.
 - haswell using linux 3.16 compiled with llvm 3.5
In all case, the program compiled and runs correctly with haswell, not
with ivybridge.

I could give a try with beignet 1.0.0, but maybe you the problem would
be obvious to you.

Any idea about the problem?

Cheers,

Nicolas Bourdaud
-------------- next part --------------
// vim: set syntax=opencl:

#define IMSTRIDE	47

inline static
float4 transform_pixel(float4 a4)
{
	float4 r4;
	int is_null;
	float C, v;

	C = a4.x - a4.y;

	is_null = isless(C, 0.5f);


	v = select(a4.z, 0.0f, is_null);

	r4.x = a4.x;
	r4.y = 255.0f*v;
	r4.z = a4.y;
	r4.w = 0.0f;

	return r4;
}


__kernel void transform(__global const uchar4* restrict in,
                        __global uchar4* restrict out)
{
	int gix = get_global_id(0);
	int giy = get_global_id(1);

	float4 pix;
	uchar4 pix_in;

	pix_in = in[gix + giy*(IMSTRIDE/sizeof(*in))];
	pix = convert_float4(pix_in);
	pix = transform_pixel(pix);
	out[gix + giy*(IMSTRIDE/sizeof(*out))] = convert_uchar4_sat(pix);
}
-------------- next part --------------
A non-text attachment was scrubbed...
Name: haswell.log
Type: text/x-log
Size: 206 bytes
Desc: not available
URL: <http://lists.freedesktop.org/archives/beignet/attachments/20141117/e23b1d9e/attachment.bin>
-------------- next part --------------
A non-text attachment was scrubbed...
Name: ivybridge.log
Type: text/x-log
Size: 714 bytes
Desc: not available
URL: <http://lists.freedesktop.org/archives/beignet/attachments/20141117/e23b1d9e/attachment-0001.bin>