From mboxrd@z Thu Jan 1 00:00:00 1970 From: bugzilla-daemon@freedesktop.org Subject: [Bug 100067] [OpenCL] const int in argument list crashes build Date: Wed, 22 Mar 2017 22:40:43 +0000 Message-ID: References: Mime-Version: 1.0 Content-Type: multipart/mixed; boundary="===============0769083249==" Return-path: 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 1BD776E9A8 for ; Wed, 22 Mar 2017 22:40:43 +0000 (UTC) In-Reply-To: List-Unsubscribe: , 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 --===============0769083249== Content-Type: multipart/alternative; boundary="14902224430.eb0Bc99.4883"; charset="UTF-8" --14902224430.eb0Bc99.4883 Date: Wed, 22 Mar 2017 22:40:43 +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=3D100067 --- Comment #5 from Mig --- minimal.cpp compiled with gcc -c minimal.cpp -g -o minimal.o [miguel@antergos-mig extra]$ gdb GNU gdb (GDB) 7.12.1 Copyright (C) 2017 Free Software Foundation, Inc. License GPLv3+: GNU GPL version 3 or later This is free software: you are free to change and redistribute it. There is NO WARRANTY, to the extent permitted by law. Type "show copying" and "show warranty" for details. This GDB was configured as "x86_64-pc-linux-gnu". Type "show configuration" for configuration details. For bug reporting instructions, please see: . Find the GDB manual and other documentation resources online at: . For help, type "help". Type "apropos word" to search for commands related to "word". (gdb) file ./minimal Reading symbols from ./minimal...done. (gdb) b 20 Breakpoint 1 at 0x400cee: file minimal.cpp, line 20. (gdb) run Starting program: /home/miguel/Dokumente/OpenCLExamples/myGEMM-master/extra/minimal=20 >>> Initializing OpenCL... [Thread debugging using libthread_db enabled] Using host libthread_db library "/usr/lib/libthread_db.so.1". [New Thread 0x7fffef7f8700 (LWP 3517)] [New Thread 0x7fffeedf2700 (LWP 3518)] [New Thread 0x7fffee5f1700 (LWP 3519)] [New Thread 0x7fffeddf0700 (LWP 3520)] [New Thread 0x7fffed5ef700 (LWP 3521)] % Device: AMD TONGA (DRM 3.9.0 / 4.10.4-1-ARCH, LLVM 3.9.1), 2046.3 MiB mem= ory, max allocation 1432.4 MiB, driver 17.0.1 Thread 1 "minimal" received signal SIGSEGV, Segmentation fault. 0x00007ffff2b9eb18 in llvm::SIInstrInfo::getInstSizeInBytes(llvm::MachineIn= str const&) const () from /usr/lib/libLLVM-3.9.so (gdb) Also when I compile minimal.cl with=20 clang -x cl -target amdgcn-- -mcpu=3Dtonga -Dcl_clang_storage_class_specifi= ers=3D1 -Xclang -mlink-bitcode-file -Xclang /usr/local/lib/clc/tonga-amdgcn--.bc -I/usr/local/include/clc -include /usr/local/include/clc/clc.h minimal.cl '+fp64-fp16-denormals' is not a recognized feature for this target (ignoring feature) '+fp64-fp16-denormals' is not a recognized feature for this target (ignoring feature) minimal.cl:2:15: error: unsupported call to function get_global_id.3 __kernel void myGEMM1(const int M,=20 ^ minimal.cl:2:15: error: unsupported call to function get_global_id.3 clang-3.9: /home/miguel/Downloads/llvm-3.9.1.src/lib/Target/AMDGPU/SIInstrInfo.cpp:242= 8: void llvm::SIInstrInfo::legalizeOperands(llvm::MachineInstr&) const: Assert= ion `MBB.getParent()->getSubtarget().getGeneration() < SISubtarget::VOLCANIC_ISLANDS && "FIXME: Need to emit flat atomics here"' failed. #0 0x00007efe68ec1662 llvm::sys::PrintStackTrace(llvm::raw_ostream&) /home/miguel/Downloads/llvm-3.9.1.src/lib/Support/Unix/Signals.inc:402:0 ... I get errors. --=20 You are receiving this mail because: You are the assignee for the bug.= --14902224430.eb0Bc99.4883 Date: Wed, 22 Mar 2017 22:40:43 +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 # 5 on bug 10006= 7 from Mig
minimal.cpp compiled with

gcc -c minimal.cpp -g   -o minimal.o

[miguel@antergos-mig extra]$ gdb
GNU gdb (GDB) 7.12.1
Copyright (C) 2017 Free Software Foundation, Inc.
License GPLv3+: GNU GPL version 3 or later <http://gnu.org/licenses/gpl.html>
This is free software: you are free to change and redistribute it.
There is NO WARRANTY, to the extent permitted by law.  Type "show copy=
ing"
and "show warranty" for details.
This GDB was configured as "x86_64-pc-linux-gnu".
Type "show configuration" for configuration details.
For bug reporting instructions, please see:
<http://www.gnu.org/so=
ftware/gdb/bugs/>.
Find the GDB manual and other documentation resources online at:
<http://www.g=
nu.org/software/gdb/documentation/>.
For help, type "help".
Type "apropos word" to search for commands related to "word&=
quot;.
(gdb) file ./minimal
Reading symbols from ./minimal...done.
(gdb) b 20
Breakpoint 1 at 0x400cee: file minimal.cpp, line 20.
(gdb) run
Starting program:
/home/miguel/Dokumente/OpenCLExamples/myGEMM-master/extra/minimal=20
>>> Initializing OpenCL...
[Thread debugging using libthread_db enabled]
Using host libthread_db library "/usr/lib/libthread_db.so.1".
[New Thread 0x7fffef7f8700 (LWP 3517)]
[New Thread 0x7fffeedf2700 (LWP 3518)]
[New Thread 0x7fffee5f1700 (LWP 3519)]
[New Thread 0x7fffeddf0700 (LWP 3520)]
[New Thread 0x7fffed5ef700 (LWP 3521)]
% Device: AMD TONGA (DRM 3.9.0 / 4.10.4-1-ARCH, LLVM 3.9.1), 2046.3 MiB mem=
ory,
max allocation 1432.4 MiB, driver  17.0.1

Thread 1 "minimal" received signal SIGSEGV, Segmentation fault.
0x00007ffff2b9eb18 in llvm::SIInstrInfo::getInstSizeInBytes(llvm::MachineIn=
str
const&) const ()
   from /usr/lib/libLLVM-3.9.so
(gdb)


Also when I compile minimal.cl with=20
clang -x cl -target amdgcn-- -mcpu=3Dtonga -Dcl_clang_storage_class_specifi=
ers=3D1
-Xclang -mlink-bitcode-file -Xclang /usr/local/lib/clc/tonga-amdgcn--.bc
-I/usr/local/include/clc -include /usr/local/include/clc/clc.h minimal.cl
'+fp64-fp16-denormals' is not a recognized feature for this target (ignoring
feature)
'+fp64-fp16-denormals' is not a recognized feature for this target (ignoring
feature)
minimal.cl:2:15: error: unsupported call to function get_global_id.3
__kernel void myGEMM1(const int M,=20
              ^
minimal.cl:2:15: error: unsupported call to function get_global_id.3
clang-3.9:
/home/miguel/Downloads/llvm-3.9.1.src/lib/Target/AMDGPU/SIInstrInfo.cpp:242=
8:
void llvm::SIInstrInfo::legalizeOperands(llvm::MachineInstr&) const: As=
sertion
`MBB.getParent()->getSubtarget<SISubtarget>().getGeneration() <
SISubtarget::VOLCANIC_ISLANDS && "FIXME: Need to emit flat ato=
mics here"'
failed.
#0 0x00007efe68ec1662 llvm::sys::PrintStackTrace(llvm::raw_ostream&)
/home/miguel/Downloads/llvm-3.9.1.src/lib/Support/Unix/Signals.inc:402:0

...

I get errors.


You are receiving this mail because:
  • You are the assignee for the bug.
= --14902224430.eb0Bc99.4883-- --===============0769083249== Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: base64 Content-Disposition: inline X19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX18KZHJpLWRldmVs IG1haWxpbmcgbGlzdApkcmktZGV2ZWxAbGlzdHMuZnJlZWRlc2t0b3Aub3JnCmh0dHBzOi8vbGlz dHMuZnJlZWRlc2t0b3Aub3JnL21haWxtYW4vbGlzdGluZm8vZHJpLWRldmVsCg== --===============0769083249==--