Quuxplusone
commented
5 years ago Attached HelloWorld.zip (3541 bytes, application/zip): OpenCL Programming Guide - Chapter 2 Exercise Code
Open Quuxplusone opened 5 years ago
Quuxplusone
commented
5 years ago Attached HelloWorld.zip (3541 bytes, application/zip): OpenCL Programming Guide - Chapter 2 Exercise Code
Quuxplusone
commented
5 years ago when I debug the "HelloWorld" with GNU debuger, The complete function call
stack information is as follows:
********************************************************************************
(gdb) bt
#0 0x0000005555936a5c in __GI_raise (sig=<optimized out>) at
../sysdeps/unix/sysv/linux/raise.c:55
#1 0x0000005555938be0 in __GI_abort () at abort.c:89
#2 0x000000555597b860 in __libc_message (do_abort=<optimized out>,
fmt=<optimized out>) at ../sysdeps/posix/libc_fatal.c:175
#3 0x000000555598c22c in malloc_printerr (ptr=<optimized out>,
str=0x5555a77f50 "free(): invalid pointer", action=3)
at malloc.c:4974
#4 _int_free (have_lock=0, p=<optimized out>, av=<optimized out>) at
malloc.c:3841
#5 __GI___libc_free (mem=<optimized out>) at malloc.c:2951
#6 0x00000055556728f0 in operator delete (ptr=<optimized out>) at
../../../../libstdc++-v3/libsupc++/del_op.cc:46
#7 0x0000005555708298 in deallocate (this=<optimized out>, __p=<optimized out>)
at /builddir/build/BUILD/gcc-4.9.3/obj-mips64el-redhat-linux/mips64el-redhat-linux/libstdc++-v3/include/ext/new_allocator.h:110
#8 std::string::_Rep::_M_destroy (this=<optimized out>, __a=...)
at /builddir/build/BUILD/gcc-4.9.3/obj-mips64el-redhat-linux/mips64el-redhat-linux/libstdc++-v3/include/bits/basic_string.tcc:449
#9 0x0000005555d3001c in std::string::_Rep::_M_dispose (this=<optimized out>,
__a=...)
at /usr/include/c++/4.9.3/bits/basic_string.h:249
#10 0x0000005555d44148 in _M_dispose (__a=..., this=<optimized out>) at
/usr/include/c++/4.9.3/bits/basic_string.h:240
#11 ~basic_string (this=0xffffff1d70, __in_chrg=<optimized out>) at
/usr/include/c++/4.9.3/bits/basic_string.h:547
#12 ParseTargetArgs (Args=..., Opts=...) at /root/rpmbuild/BUILD/cfe-
3.8.1.src/lib/Frontend/CompilerInvocation.cpp:2034
#13 clang::CompilerInvocation::CreateFromArgs (Res=..., ArgBegin=0x120098570,
ArgEnd=<optimized out>, Diags=...)
at /root/rpmbuild/BUILD/cfe-3.8.1.src/lib/Frontend/CompilerInvocation.cpp:2072
#14 0x0000005555b46a44 in (anonymous namespace)::compile_llvm (llvm_ctx=...,
source="\n__kernel void hello_kernel(__global const float *a,\n\t\t\t\t\t\t__global const float *b,\n\t\t\t\t\t\t__global float *result)\n{\n int gid = get_global_id(0);\n\n result[gid] = a[gid] + b[gid];\n}\n",
headers=std::vector of length 0, capacity 0, name="input.cl", triple="r600--", processor="caicos", opts="",
address_spaces=..., optimization_level=@0xffffff3a88: 1437349920, r_log="") at llvm/invocation.cpp:179
#15 0x0000005555b4806c in clover::compile_program_llvm (
source="\n__kernel void hello_kernel(__global const float *a,\n\t\t\t\t\t\t__global const float *b,\n\t\t\t\t\t\t__global float *result)\n{\n int gid = get_global_id(0);\n\n result[gid] = a[gid] + b[gid];\n}\n",
---Type <return> to continue, or q <return> to quit---
headers=std::vector of length 0, capacity 0, ir=<optimized out>, target="caicos-r600--", opts="", r_log="")
at llvm/invocation.cpp:864
#16 0x0000005555b3c7a8 in clover::program::build (this=0x120093060, devs=...,
opts=0x5555b9c528 "",
headers=std::vector of length 0, capacity 0) at core/program.cpp:63
#17 0x0000005555b1fa68 in clBuildProgram (d_prog=<optimized out>,
num_devs=<optimized out>, d_devs=0x0, p_opts=<optimized out>,
pfn_notify=0x0, user_data=0x0) at api/program.cpp:184
#18 0x00000055555ee4ac in clBuildProgram (program=0x120093068,
num_devices=<optimized out>, device_list=0x0, options=0x0,
pfn_notify=0x0, user_data=<optimized out>) at ocl_icd_loader_gen.c:386
#19 0x0000000120001d8c in CreateProgram (context=0x120018018,
device=0x120041d08, fileName=0x120002e68 "HelloWorld.cl")
at /root/TarAll/src/Chapter_2/HelloWorld/HelloWorld.cpp:158
#20 0x00000001200022f8 in main (argc=1, argv=0xffffffb3a8) at
/root/TarAll/src/Chapter_2/HelloWorld/HelloWorld.cpp:255
********************************************************************************
I noticed the Frame 12, Further information is shown below:
static void ParseTargetArgs(TargetOptions &Opts, ArgList &Args) {
2024 using namespace options;
2025 Opts.ABI = Args.getLastArgValue(OPT_target_abi);
2026 Opts.CPU = Args.getLastArgValue(OPT_target_cpu);
2027 Opts.FPMath = Args.getLastArgValue(OPT_mfpmath);
2028 Opts.FeaturesAsWritten = Args.getAllArgValues(OPT_target_feature);
2029 Opts.LinkerVersion = Args.getLastArgValue(OPT_target_linker_version);
2030 Opts.Triple = llvm::Triple::normalize(Args.getLastArgValue(OPT_triple));
2031 Opts.Reciprocals = Args.getAllArgValues(OPT_mrecip_EQ);
2032 // Use the default target triple if unspecified.
2033 if (Opts.Triple.empty())
2034 Opts.Triple = llvm::sys::getDefaultTargetTriple();
2035 }
In order to get default Triple, the function
“llvm::sys::getDefaultTargetTriple()” was called and a c++ string "mips64el-
redhat-linux" returned, After the assignment to the variable -- Opts.Triple--
is completed, the program crashes.When I compiled the clang package, the following warning message reported.
Figuring out the warnings would be my job this Saturday.
***********************************************************************
[root@localhost SPECS]# rpmbuild -bb clang.spec
Executing(%prep): /bin/sh -e /var/tmp/rpm-tmp.viOlsk
+ umask 022
+ cd /root/rpmbuild/BUILD
+ cd /root/rpmbuild/BUILD
+ rm -rf cfe-3.8.1.src
+ /usr/bin/xz -dc /root/rpmbuild/SOURCES/cfe-3.8.1.src.tar.xz
+ /usr/bin/tar -xf -
+ STATUS=0
+ '[' 0 -ne 0 ']'
+ cd cfe-3.8.1.src
+ /usr/bin/chmod -Rf a+rX,u+w,g-w,o-w .
+ echo 'Patch #0 (0001-GCC-PR23529-Sema-part-of-attrbute-abi_tag-
support.patch):'
Patch #0 (0001-GCC-PR23529-Sema-part-of-attrbute-abi_tag-support.patch):
+ /usr/bin/cat /root/rpmbuild/SOURCES/0001-GCC-PR23529-Sema-part-of-attrbute-
abi_tag-support.patch
+ /usr/bin/patch -p1 --fuzz=0
patching file docs/ItaniumMangleAbiTags.rst
patching file docs/index.rst
patching file include/clang/Basic/Attr.td
patching file include/clang/Basic/AttrDocs.td
patching file include/clang/Basic/DiagnosticSemaKinds.td
patching file include/clang/Sema/AttributeList.h
patching file lib/Sema/SemaDecl.cpp
patching file lib/Sema/SemaDeclAttr.cpp
patching file test/SemaCXX/attr-abi-tag-syntax.cpp
+ echo 'Patch #1 (0002-GCC-PR23529-Mangler-part-of-attrbute-abi_tag-
support.patch):'
Patch #1 (0002-GCC-PR23529-Mangler-part-of-attrbute-abi_tag-support.patch):
+ /usr/bin/cat /root/rpmbuild/SOURCES/0002-GCC-PR23529-Mangler-part-of-attrbute-
abi_tag-support.patch
+ /usr/bin/patch -p1 --fuzz=0
patching file lib/AST/ItaniumMangle.cpp
patching file lib/Sema/SemaDeclAttr.cpp
patching file test/CodeGenCXX/mangle-abi-tag.cpp
patching file test/SemaCXX/attr-abi-tag-syntax.cpp
+ echo 'Patch #10 (clang-cs2c-toolchains.patch):'
Patch #10 (clang-cs2c-toolchains.patch):
+ /usr/bin/cat /root/rpmbuild/SOURCES/clang-cs2c-toolchains.patch
+ /usr/bin/patch -p1 --fuzz=0
patching file lib/Driver/ToolChains.cpp
+ echo 'Patch #11 (0003-cfe-path_max.patch):'
Patch #11 (0003-cfe-path_max.patch):
+ /usr/bin/cat /root/rpmbuild/SOURCES/0003-cfe-path_max.patch
+ /usr/bin/patch -p2 --fuzz=0
patching file lib/Basic/FileManager.cpp
+ echo 'Patch #12 (0001-clang-has_feature.patch):'
Patch #12 (0001-clang-has_feature.patch):
+ /usr/bin/cat /root/rpmbuild/SOURCES/0001-clang-has_feature.patch
+ /usr/bin/patch -p2 --fuzz=0
patching file lib/Headers/stddef.h
+ echo 'Patch #13 (0002-clang-defTriple.patch):'
Patch #13 (0002-clang-defTriple.patch):
+ /usr/bin/cat /root/rpmbuild/SOURCES/0002-clang-defTriple.patch
+ /usr/bin/patch -p2 --fuzz=0
patching file include/clang/Basic/TargetOptions.h
patching file lib/Basic/Version.cpp
patching file lib/Frontend/CompilerInvocation.cpp
+ exit 0
Executing(%build): /bin/sh -e /var/tmp/rpm-tmp.D42iry
+ umask 022
+ cd /root/rpmbuild/BUILD
+ cd cfe-3.8.1.src
+ mkdir -p _build
+ cd _build
+ CFLAGS='-O3 -g -march=loongson3a -mabi=64'
+ export CFLAGS
+ CXXFLAGS='-O3 -g -march=loongson3a -mabi=64'
+ export CXXFLAGS
+ FFLAGS='-O3 -g -march=loongson3a -mabi=64 -I/usr/lib64/gfortran/modules'
+ export FFLAGS
+ FCFLAGS='-O3 -g -march=loongson3a -mabi=64 -I/usr/lib64/gfortran/modules'
+ export FCFLAGS
+ LDFLAGS='-Wl,-z,relro '
+ export LDFLAGS
+ /usr/bin/cmake -DCMAKE_C_FLAGS_RELEASE:STRING=-DNDEBUG -
DCMAKE_CXX_FLAGS_RELEASE:STRING=-DNDEBUG -DCMAKE_Fortran_FLAGS_RELEASE:STRING=-
DNDEBUG -DCMAKE_VERBOSE_MAKEFILE:BOOL=ON -DCMAKE_INSTALL_PREFIX:PATH=/usr -
DINCLUDE_INSTALL_DIR:PATH=/usr/include -DLIB_INSTALL_DIR:PATH=/usr/lib64 -
DSYSCONF_INSTALL_DIR:PATH=/etc -DSHARE_INSTALL_PREFIX:PATH=/usr/share -
DLIB_SUFFIX=64 -DBUILD_SHARED_LIBS:BOOL=ON .. -DLLVM_LINK_LLVM_DYLIB:BOOL=ON -
DCMAKE_BUILD_TYPE=RelWithDebInfo -DLLVM_CONFIG:FILEPATH=/usr/bin/llvm-config-64
-DCLANG_ENABLE_ARCMT:BOOL=ON -DCLANG_ENABLE_STATIC_ANALYZER:BOOL=ON -
DCLANG_INCLUDE_DOCS:BOOL=ON -DCLANG_INCLUDE_TESTS:BOOL=ON -
DCLANG_PLUGIN_SUPPORT:BOOL=ON -DCLANG_BUILD_EXAMPLES:BOOL=OFF -DLIB_SUFFIX=
-- The C compiler identification is GNU 4.9.3
-- The CXX compiler identification is GNU 4.9.3
-- Check for working C compiler: /usr/lib64/ccache/cc
-- Check for working C compiler: /usr/lib64/ccache/cc -- works
-- Detecting C compiler ABI info
-- Detecting C compiler ABI info - done
-- Detecting C compile features
-- Detecting C compile features - done
-- Check for working CXX compiler: /usr/lib64/ccache/c++
-- Check for working CXX compiler: /usr/lib64/ccache/c++ -- works
-- Detecting CXX compiler ABI info
-- Detecting CXX compiler ABI info - done
-- Detecting CXX compile features
-- Detecting CXX compile features - done
-- Found LLVM_CONFIG as /usr/bin/llvm-config-64
-- Performing Test C_SUPPORTS_FPIC
-- Performing Test C_SUPPORTS_FPIC - Success
-- Performing Test CXX_SUPPORTS_FPIC
-- Performing Test CXX_SUPPORTS_FPIC - Success
-- Building with -fPIC
-- Performing Test SUPPORTS_FVISIBILITY_INLINES_HIDDEN_FLAG
-- Performing Test SUPPORTS_FVISIBILITY_INLINES_HIDDEN_FLAG - Success
-- Performing Test C_SUPPORTS_WERROR_DATE_TIME
-- Performing Test C_SUPPORTS_WERROR_DATE_TIME - Success
-- Performing Test CXX_SUPPORTS_WERROR_DATE_TIME
-- Performing Test CXX_SUPPORTS_WERROR_DATE_TIME - Success
-- Performing Test CXX_SUPPORTS_CXX11
-- Performing Test CXX_SUPPORTS_CXX11 - Success
-- Performing Test C_SUPPORTS_FNO_FUNCTION_SECTIONS
-- Performing Test C_SUPPORTS_FNO_FUNCTION_SECTIONS - Success
-- Performing Test C_SUPPORTS_FFUNCTION_SECTIONS
-- Performing Test C_SUPPORTS_FFUNCTION_SECTIONS - Success
-- Performing Test CXX_SUPPORTS_FFUNCTION_SECTIONS
-- Performing Test CXX_SUPPORTS_FFUNCTION_SECTIONS - Success
-- Performing Test C_SUPPORTS_FDATA_SECTIONS
-- Performing Test C_SUPPORTS_FDATA_SECTIONS - Success
-- Performing Test CXX_SUPPORTS_FDATA_SECTIONS
-- Performing Test CXX_SUPPORTS_FDATA_SECTIONS - Success
-- Found PythonInterp: /usr/bin/python2.7 (found version "2.7.8")
-- Clang version: 3.8.1
-- Performing Test CXX_SUPPORTS_NO_NESTED_ANON_TYPES_FLAG
-- Performing Test CXX_SUPPORTS_NO_NESTED_ANON_TYPES_FLAG - Failed
-- Configuring done
CMake Warning (dev) at /usr/share/llvm/cmake/AddLLVM.cmake:513
(add_dependencies):
Policy CMP0046 is not set: Error on non-existent dependency in
add_dependencies. Run "cmake --help-policy CMP0046" for policy details.
Use the cmake_policy command to set the policy and suppress this warning.
The dependency target "intrinsics_gen" of target "clangFrontend" does not
exist.
Call Stack (most recent call first):
CMakeLists.txt:396 (llvm_add_library)
lib/Frontend/CMakeLists.txt:9 (add_clang_library)
This warning is for project developers. Use -Wno-dev to suppress it.
-- Generating done
CMake Warning:
Manually-specified variables were not used by the project:
CMAKE_CXX_FLAGS_RELEASE
CMAKE_C_FLAGS_RELEASE
CMAKE_Fortran_FLAGS_RELEASE
INCLUDE_INSTALL_DIR
LIB_INSTALL_DIR
LIB_SUFFIX
SHARE_INSTALL_PREFIX
SYSCONF_INSTALL_DIRUnfortunately I can not reproduce the bug on the recent version of LLVM/Clang because I have no access to MIPS host with appropriate video subsystem. LLVM/Clang 3.8 was released three years ago. Could you check the problem using LLVM/Clang 7.x or 8.x?
Quuxplusone
commented
5 years ago @Simon Atanasyan
Many thanks for your advices. As you can see from Mesa's rpmbuild SPEC file,
there is a compilation dependency between the Mesa package and llvm/clang, as
shown below.
This compilation dependency causes the high version of the mesa package to be
compiled, while the early compilations such as "libclc", "clinfo", and "ocl-
icd" will not be available, and there is also no way to accurately determine
the version of Mesa that need to compile.
***********************************************************
#setction of mesa.spec
%if 0%{?with_llvm}
%if 0%{?with_private_llvm}
BuildRequires: mesa-private-llvm-devel
%else
BuildRequires: llvm-devel >= 3.5.0
%if 0%{?with_opencl}
BuildRequires: clang-devel >= 3.0
%endif
%endif
%endif
***********************************************************
At 11 o'clock last night, I completed the compilation of llvm-clang 8.0 and
started to compile the mesa 11 package according to your suggestions. However,
under the Fedora 21 system, there are too many mesa API compatibility issues,
one of which is shown below, and because the mesa needs to be recompiled, the
number of available Openc Platform returned by the clinfo command is 0.
***********************************************************
#The llvm 8.0
[root@localhost ~]# llc -version
LLVM (http://llvm.org/):
LLVM version 8.0.0
Optimized build.
Default target: mips64el-redhat-linux
Host CPU: (unknown)
Registered Targets:
amdgcn - AMD GCN GPUs
mips - MIPS (32-bit big endian)
mips64 - MIPS (64-bit big endian)
mips64el - MIPS (64-bit little endian)
mipsel - MIPS (32-bit little endian)
nvptx - NVIDIA PTX 32-bit
nvptx64 - NVIDIA PTX 64-bit
r600 - AMD GPUs HD2XXX-HD6XXX
***********************************************************
#The clang 8.0
[root@localhost ~]# clang++ --version
clang version 8.0.0
Target: mips64el-redhat-linux
Thread model: posix
InstalledDir: /usr/bin
***********************************************************
#Compatibility issues with mesa and llvm api versions
In file included from draw/draw_llvm.c:45:0:
./gallivm/lp_bld_intr.h:63:20: error: unknown type name 'LLVMAttribute'
LLVMAttribute attr);
^
draw/draw_llvm.c: In function 'create_jit_sampler_type':
draw/draw_llvm.c:178:22: warning: unused variable 'target' [-Wunused-variable]
LLVMTargetDataRef target = gallivm->target;
^
draw/draw_llvm.c: In function 'create_jit_context_type':
draw/draw_llvm.c:218:22: warning: unused variable 'target' [-Wunused-variable]
LLVMTargetDataRef target = gallivm->target;
^
draw/draw_llvm.c: In function 'create_jit_vertex_header':
draw/draw_llvm.c:377:22: warning: unused variable 'target' [-Wunused-variable]
LLVMTargetDataRef target = gallivm->target;
^
draw/draw_llvm.c: In function 'draw_llvm_generate':
draw/draw_llvm.c:1580:10: error: implicit declaration of function
'LLVMAddAttribute' [-Werror=implicit-function-declaration]
LLVMAddAttribute(LLVMGetParam(variant_func, i),
^
draw/draw_llvm.c:1581:27: error: 'LLVMNoAliasAttribute' undeclared (first use
in this function)
LLVMNoAliasAttribute);
^
draw/draw_llvm.c:1581:27: note: each undeclared identifier is reported only
once for each function it appears in
draw/draw_llvm.c: In function 'draw_gs_llvm_generate':
draw/draw_llvm.c:2123:27: error: 'LLVMNoAliasAttribute' undeclared (first use
in this function)
LLVMNoAliasAttribute);
^
cc1: some warnings being treated as errors
Makefile:2115: recipe for target 'draw/draw_llvm.lo' failed
make[3]: *** [draw/draw_llvm.lo] Error 1
make[3]: *** Waiting for unfinished jobs....
make[3]: Leaving directory '/root/rpmbuild/BUILD/mesa-
20151218/src/gallium/auxiliary'
Makefile:580: recipe for target 'all-recursive' failed
make[2]: *** [all-recursive] Error 1
make[2]: Leaving directory '/root/rpmbuild/BUILD/mesa-20151218/src/gallium'
Makefile:674: recipe for target 'all-recursive' failed
make[1]: *** [all-recursive] Error 1
make[1]: Leaving directory '/root/rpmbuild/BUILD/mesa-20151218/src'
Makefile:619: recipe for target 'all-recursive' failed
make: *** [all-recursive] Error 1
error: Bad exit status from /var/tmp/rpm-tmp.wvfWMM (%build)
RPM build errors:
Bad exit status from /var/tmp/rpm-tmp.wvfWMM (%build)
***********************************************************
#The number of OpenCL platfoms
[root@localhost SPECS]# clinfo
Number of platforms 0
***********************************************************
[root@localhost SPECS]# rpm -qa | grep libOpenCL
mesa-libOpenCL-devel-11.1.0-5.20151218.fc21.loongson.6.mips64el
mesa-libOpenCL-11.1.0-5.20151218.fc21.loongson.6.mips64el
[root@localhost SPECS]# yum info mesa-libOpenCL
Loaded plugins: auto-update-debuginfo, langpacks
Installed Packages
Name : mesa-libOpenCL
Arch : mips64el
Version : 11.1.0
Release : 5.20151218.fc21.loongson.6
Size : 1.0 M
Repo : installed
From repo : /mesa-libOpenCL-11.1.0-5.20151218.fc21.loongson.6.mips64el
Summary : Mesa OpenCL runtime library
URL : http://www.mesa3d.org
License : MIT
Description : Mesa OpenCL runtime library.@Simon Atanasyan
To be honest, this above problem with the Mesa 11 package and is caused by upgrading llvm. Which is the just version of mesa that matches llvm8.0, so that the OpenCL development environment can be successfully built on the Fedora 21 platform.
For the "Free invalid pointer" problem of clang 3.8.1 mentioned in the previous comment, I made the following changes to the source code by patching:
**************************************************************************
/* Create a default constructor for the TargetOptions class on the mips64el
platform, and skip the assignment to Opts.Triple by macro detection in the
ParseTargetArgs function of the file CompilerInvocation.cpp.*/
diff -Nuar a/cfe-3.8.1.src/include/clang/Basic/TargetOptions.h b/cfe-
3.8.1.src/include/clang/Basic/TargetOptions.h
--- a/cfe-3.8.1.src/include/clang/Basic/TargetOptions.h 2015-06-11
10:53:41.000000000 -0400
+++ b/cfe-3.8.1.src/include/clang/Basic/TargetOptions.h 2019-07-09
11:29:00.359434024 -0400
@@ -47,6 +47,9 @@
std::vector<std::string> Features;
std::vector<std::string> Reciprocals;
+#if defined(__mips64) && defined(_LP64)
+ TargetOptions():Triple("mips64el-redhat-linux"){};
+#endif
};
} // end namespace clang
diff -Nuar a/cfe-3.8.1.src/lib/Frontend/CompilerInvocation.cpp b/cfe-
3.8.1.src/lib/Frontend/CompilerInvocation.cpp
--- a/cfe-3.8.1.src/lib/Frontend/CompilerInvocation.cpp 2016-01-12
16:01:56.000000000 -0500
+++ b/cfe-3.8.1.src/lib/Frontend/CompilerInvocation.cpp 2019-07-09
11:31:14.402400117 -0400
@@ -44,6 +44,7 @@
#include <memory>
#include <sys/stat.h>
#include <system_error>
+#include <iostream>
using namespace clang;
//===----------------------------------------------------------------------===//
@@ -2027,11 +2028,14 @@
Opts.FPMath = Args.getLastArgValue(OPT_mfpmath);
Opts.FeaturesAsWritten = Args.getAllArgValues(OPT_target_feature);
Opts.LinkerVersion = Args.getLastArgValue(OPT_target_linker_version);
- Opts.Triple = llvm::Triple::normalize(Args.getLastArgValue(OPT_triple));
Opts.Reciprocals = Args.getAllArgValues(OPT_mrecip_EQ);
+#if !(defined(__mips64) && defined(_LP64))
+ Opts.Triple = llvm::Triple::normalize(Args.getLastArgValue(OPT_triple));
// Use the default target triple if unspecified.
if (Opts.Triple.empty())
- Opts.Triple = llvm::sys::getDefaultTargetTriple();
+ Opts.Triple = llvm::sys::getDefaultTargetTriple();
+#endif
+ std::cout << "Opts.Triple is: " << Opts.Triple << std::endl;
}
**************************************************************************
Although the above modification is not flexible enough, it solves the problem
of Triple parsing, and the compilation process begins to enter the
CodeGeneration phase.
Although the above modification is not flexible enough, it solves the problem
of Triple parsing, and the compilation process begins to enter the
CodeGeneration phase. The new problems that come with it are as follows: The
complete GDB stack information is shown below:
**************************************************************************
#0 0x0000005555936a5c in __GI_raise (sig=<optimized out>) at
../sysdeps/unix/sysv/linux/raise.c:55
#1 0x0000005555938be0 in __GI_abort () at abort.c:89
#2 0x000000555597b860 in __libc_message (do_abort=<optimized out>,
fmt=<optimized out>) at ../sysdeps/posix/libc_fatal.c:175
#3 0x000000555598c22c in malloc_printerr (ptr=<optimized out>,
str=0x5555a77f50 "free(): invalid pointer", action=3)
at malloc.c:4974
#4 _int_free (have_lock=0, p=<optimized out>, av=<optimized out>) at
malloc.c:3841
#5 __GI___libc_free (mem=<optimized out>) at malloc.c:2951
#6 0x000000555888df00 in operator delete(void*) () from /lib64/libLLVM-3.8.so
#7 0x00000055588fe004 in std::string::_M_mutate(unsigned long, unsigned long,
unsigned long) () from /lib64/libLLVM-3.8.so
#8 0x0000005558908214 in std::string::replace(unsigned long, unsigned long,
char const*, unsigned long) ()
from /lib64/libLLVM-3.8.so
#9 0x00000055577307e0 in replace (__k2=<optimized out>, __k1=<optimized out>,
__i2=..., __i1=..., this=0x1200f8aa8)
at /usr/include/c++/4.9.3/bits/basic_string.h:1671
#10 assign<char const*> (__last=<optimized out>, __first=<optimized out>,
this=0x1200f8aa8)
at /usr/include/c++/4.9.3/bits/basic_string.h:1176
#11 llvm::Timer::init (this=0x1200f8a68, N=..., tg=...) at
/root/rpmbuild/BUILD/llvm-3.8.1.src/lib/Support/Timer.cpp:104
#12 0x0000005557730864 in llvm::Timer::init (this=0x1200f8a68, N=...)
at /root/rpmbuild/BUILD/llvm-3.8.1.src/lib/Support/Timer.cpp:99
#13 0x0000005556279300 in Timer (N=..., this=0x1200f8a68) at
/usr/include/llvm/Support/Timer.h:88
#14 BackendConsumer (CoverageInfo=0x0, C=..., OS=<optimized out>,
LinkModules=..., InFile="input.cl", TimePasses=false,
LangOpts=..., TargetOpts=..., CodeGenOpts=..., PPOpts=..., HeaderSearchOpts=..., Diags=..., Action=clang::Backend_EmitNothing,
this=0x1200f8a20) at /root/rpmbuild/BUILD/cfe-3.8.1.src/lib/CodeGen/CodeGenAction.cpp:78
#15 clang::CodeGenAction::CreateASTConsumer (this=0xffffff2db0, CI=...,
InFile=...)
at /root/rpmbuild/BUILD/cfe-3.8.1.src/lib/CodeGen/CodeGenAction.cpp:723
#16 0x0000005555d5904c in clang::FrontendAction::CreateWrappedASTConsumer
(this=<optimized out>, CI=..., InFile=...)
at /root/rpmbuild/BUILD/cfe-3.8.1.src/lib/Frontend/FrontendAction.cpp:140
#17 0x0000005555d5a7a0 in clang::FrontendAction::BeginSourceFile
(this=<optimized out>, CI=..., Input=...)
at /root/rpmbuild/BUILD/cfe-3.8.1.src/lib/Frontend/FrontendAction.cpp:319
#18 0x0000005555d28678 in clang::CompilerInstance::ExecuteAction
(this=0xffffff2ca0, Act=...)
at /root/rpmbuild/BUILD/cfe-3.8.1.src/lib/Frontend/CompilerInstance.cpp:839
#19 0x0000005555b4710c in (anonymous namespace)::compile_llvm (llvm_ctx=...,
source="\n__kernel void hello_kernel(__global const float *a,\n\t\t\t\t\t\t__global const float *b,\n\t\t\t\t\t\t__global float *result)\n{\n int gid = get_global_id(0);\n\n result[gid] = a[gid] + b[gid];\n}\n",
headers=std::vector of length 0, capacity 0, name="input.cl", triple="r600--", processor="caicos", opts="",
address_spaces=..., optimization_level=@0xffffff3a88: 2, r_log="") at llvm/invocation.cpp:259
#20 0x0000005555b4809c in clover::compile_program_llvm (
source="\n__kernel void hello_kernel(__global const float *a,\n\t\t\t\t\t\t__global const float *b,\n\t\t\t\t\t\t__global float *result)\n{\n int gid = get_global_id(0);\n\n result[gid] = a[gid] + b[gid];\n}\n",
headers=std::vector of length 0, capacity 0, ir=<optimized out>, target="caicos-r600--", opts="", r_log="")
at llvm/invocation.cpp:864
#21 0x0000005555b3c7d8 in clover::program::build (this=0x120093090, devs=...,
opts=0x5555b9c558 "",
headers=std::vector of length 0, capacity 0) at core/program.cpp:63
#22 0x0000005555b1fa98 in clBuildProgram (d_prog=<optimized out>,
num_devs=<optimized out>, d_devs=0x0, p_opts=<optimized out>,
pfn_notify=0x0, user_data=0x0) at api/program.cpp:184
#23 0x00000055555ee4ac in clBuildProgram (program=0x120093098,
num_devices=<optimized out>, device_list=0x0, options=0x0,
pfn_notify=0x0, user_data=<optimized out>) at ocl_icd_loader_gen.c:386
#24 0x0000000120001d8c in CreateProgram (context=0x120018018,
device=0x120041d38, fileName=0x120002e68 "HelloWorld.cl")
at /root/TarAll/src/Chapter_2/HelloWorld/HelloWorld.cpp:158
#25 0x00000001200022f8 in main (argc=1, argv=0xffffffb3a8) at
/root/TarAll/src/Chapter_2/HelloWorld/HelloWorld.cpp:255
In response to the above questions, I am still doing source code analysis,
trying to solve this problem. Can you give me some good tips? Thanks again.All crashes are related to libstdc++ and unrelated to Mesa and/or OpenCL. Can
you:
a) Compile any trivial C++ "hello world" application like below using clang
3.8.1?
#include <iostream>
using namespace std;
int main()
{
cout << "Hello, World!";
return 0;
}
b) Build Clang 8.0 and compile the same trivial application?Thank you very much for your suggestion. I have never doubted that libstdc++
will have problems. Just because graduated from college， my teacher tole me a
"Truth" that the probability of a bug found in the C library code is almost
zero. Meantime, this sentence also hampers my thinking.
Compile the C++ Hello World program with a and b respectively. The compilation
steps and results are as follows:
***********************clang 3.8.1 compiling log***********************
#1.vresion info
[root@localhost llvm-compile-procedure]# clang --version
clang version 3.8.1 (tags/RELEASE_381/final)
Target: mips64el-redhat-linux
Thread model: posix
InstalledDir: /usr/bin
[root@localhost llvm-compile-procedure]# clang++ --version
clang version 3.8.1 (tags/RELEASE_381/final)
Target: mips64el-redhat-linux
Thread model: posix
InstalledDir: /usr/bin
***********************************************************************
#2.Print Compile phases
[root@localhost llvm-compile-procedure]# clang -ccc-print-phases Hello.cpp
0: input, "Hello.cpp", c++
1: preprocessor, {0}, c++-cpp-output
2: compiler, {1}, ir
3: backend, {2}, assembler
4: assembler, {3}, object
5: linker, {4}, image
***********************************************************************
#3. Internal operation command
[root@localhost llvm-compile-procedure]# clang -### Hello.cpp -o Hello.o
clang version 3.8.1 (tags/RELEASE_381/final)
Target: mips64el-redhat-linux
Thread model: posix
InstalledDir: /usr/bin
"/usr/bin/clang-3.8" "-cc1" "-triple" "mips64el-redhat-linux" "-S" "-disable-free" "-disable-llvm-verifier" "-main-file-name" "Hello.cpp" "-mrelocation-model" "static" "-mthread-model" "posix" "-mdisable-fp-elim" "-fmath-errno" "-no-integrated-as" "-mconstructor-aliases" "-fuse-init-array" "-target-cpu" "mips64r2" "-target-abi" "n64" "-mfloat-abi" "hard" "-dwarf-column-info" "-debugger-tuning=gdb" "-resource-dir" "/usr/bin/../lib64/clang/3.8.1" "-c-isystem" "." "-c-isystem" "/usr/include/c++/4.9.3/mips64el-redhat-linux" "-c-isystem" "/usr/include/c++/4.9.3" "-cxx-isystem" "." "-cxx-isystem" "/usr/include/c++/4.9.3/mips64el-redhat-linux" "-cxx-isystem" "/usr/include/c++/4.9.3" "-internal-isystem" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../include/c++/4.9.3" "-internal-isystem" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../include/c++/4.9.3/mips64el-redhat-linux" "-internal-isystem" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../include/c++/4.9.3/backward" "-internal-isystem" "/usr/local/include" "-internal-isystem" "/usr/bin/../lib64/clang/3.8.1/include" "-internal-externc-isystem" "/include" "-internal-externc-isystem" "/usr/include" "-fdeprecated-macro" "-fno-dwarf-directory-asm" "-fdebug-compilation-dir" "/root/TarAll/llvm-compile-procedure" "-ferror-limit" "19" "-fmessage-length" "132" "-fobjc-runtime=gcc" "-fcxx-exceptions" "-fexceptions" "-fdiagnostics-show-option" "-fcolor-diagnostics" "-o" "/tmp/Hello-4888b6.s" "-x" "c++" "Hello.cpp"
"/usr/bin/as" "-march" "mips64r2" "-mabi" "64" "-mno-shared" "-KPIC" "-EL" "-o" "/tmp/Hello-c5d20e.o" "/tmp/Hello-4888b6.s"
"/usr/bin/ld" "--eh-frame-hdr" "-m" "elf64ltsmip" "-dynamic-linker" "/lib64/ld-musl-mipsel.so.1" "-o" "Hello.o" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../lib64/crt1.o" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../lib64/crti.o" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/crtbegin.o" "-L/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3" "-L/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../lib64" "-L/usr/bin/../lib64" "-L/lib/../lib64" "-L/usr/lib/../lib64" "-L/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3" "-L/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../.." "-L/usr/bin/../lib" "-L/lib" "-L/usr/lib" "/tmp/Hello-c5d20e.o" "-lgcc" "--as-needed" "-lgcc_s" "--no-as-needed" "-lc" "-lgcc" "--as-needed" "-lgcc_s" "--no-as-needed" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/crtend.o" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../lib64/crtn.o"
***********************************************************************
#4. Preprocess stage
[root@localhost llvm-compile-procedure]# clang++ -E Hello.cpp
[root@localhost llvm-compile-procedure]# echo $?
0
***********************************************************************
#5. Lexical Analysis
[root@localhost llvm-compile-procedure]# clang++ -fmodules -fsyntax-only -
Xclang -dump-tokens Hello.cpp
[root@localhost llvm-compile-procedure]# echo $?
0
***********************************************************************
#6. Semantic Analysis
[root@localhost llvm-compile-procedure]# clang++ -fmodules -fsyntax-only -
Xclang -ast-dump Hello.cpp
[root@localhost llvm-compile-procedure]# echo $?
0
***********************************************************************
#7. Code Generation(Generate an IR code with a .bc and a .ll suffix)
[root@localhost llvm-compile-procedure]# clang++ -emit-llvm -c Hello.cpp -o
Hello.bc
Opts.Triple is: mips64el-redhat-linux
[root@localhost llvm-compile-procedure]# ls Hello.bc
Hello.bc
[root@localhost llvm-compile-procedure]# file Hello.bc
Hello.bc: LLVM IR bitcode
[root@localhost llvm-compile-procedure]# clang++ -O3 -S -emit-llvm Hello.cpp -o
Hello.ll
Opts.Triple is: mips64el-redhat-linux
[root@localhost llvm-compile-procedure]# file Hello.ll
Hello.ll: C source, ASCII text, with very long lines
***********************************************************************
#8. Assemble Code
clang++ -S Hello.cpp -o Hello.s
***********************************************************************
#9. Generate executables and run
[root@localhost llvm-compile-procedure]# clang++ -g -o Hello Hello.cpp
Opts.Triple is: mips64el-redhat-linux
[root@localhost llvm-compile-procedure]# ./Hello
-bash: ./Hello: /lib64/ld-musl-mipsel.so.1: bad ELF interpreter: No such file
or directory
***********************************************************************
#10. Simplify the above [4-9] stages
clang++ -save-temps Hello.cpp -o Hello
***********************clang 8.0.0 compiling log***********************
#1. clang version info
[root@localhost Hello]# clang --version
clang version 8.0.0
Target: mips64el-redhat-linux
Thread model: posix
InstalledDir: /usr/bin
[root@localhost Hello]# clang++ --version
clang version 8.0.0
Target: mips64el-redhat-linux
Thread model: posix
InstalledDir: /usr/bin
***********************************************************************
#2.Print Compile phases
[root@localhost Hello]# clang -ccc-print-phases Hello.cpp
0: input, "Hello.cpp", c++
1: preprocessor, {0}, c++-cpp-output
2: compiler, {1}, ir
3: backend, {2}, assembler
4: assembler, {3}, object
5: linker, {4}, image
***********************************************************************
#3. Internal operation command
[root@localhost Hello]# clang -### Hello.cpp -o Hello.o
clang version 8.0.0
Target: mips64el-redhat-linux
Thread model: posix
InstalledDir: /usr/bin
"/usr/bin/clang-8" "-cc1" "-triple" "mips64el-redhat-linux" "-emit-obj" "-mrelax-all" "-disable-free" "-disable-llvm-verifier" "-discard-value-names" "-main-file-name" "Hello.cpp" "-mrelocation-model" "pic" "-pic-level" "1" "-mthread-model" "posix" "-mdisable-fp-elim" "-fmath-errno" "-masm-verbose" "-mconstructor-aliases" "-fuse-init-array" "-target-cpu" "mips64r2" "-target-feature" "-noabicalls" "-target-abi" "n64" "-mfloat-abi" "hard" "-dwarf-column-info" "-debugger-tuning=gdb" "-resource-dir" "/usr/lib64/clang/8.0.0" "-c-isystem" "." "-c-isystem" "/usr/include/c++/4.9.3/mips64el-redhat-linux" "-c-isystem" "/usr/include/c++/4.9.3" "-cxx-isystem" "." "-cxx-isystem" "/usr/include/c++/4.9.3/mips64el-redhat-linux" "-cxx-isystem" "/usr/include/c++/4.9.3" "-internal-isystem" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../include/c++/4.9.3" "-internal-isystem" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../include/c++/4.9.3/mips64el-redhat-linux" "-internal-isystem" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../include/c++/4.9.3/backward" "-internal-isystem" "/usr/local/include" "-internal-isystem" "/usr/lib64/clang/8.0.0/include" "-internal-externc-isystem" "/include" "-internal-externc-isystem" "/usr/include" "-fdeprecated-macro" "-fdebug-compilation-dir" "/root/TarAll/llvm-compile-procedure/Hello" "-ferror-limit" "19" "-fmessage-length" "132" "-fobjc-runtime=gcc" "-fcxx-exceptions" "-fexceptions" "-fdiagnostics-show-option" "-fcolor-diagnostics" "-o" "/tmp/Hello-99daa5.o" "-x" "c++" "Hello.cpp" "-faddrsig"
"/usr/bin/ld" "--eh-frame-hdr" "-m" "elf64ltsmip" "-dynamic-linker" "/lib64/ld.so.1" "-o" "Hello.o" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../lib64/crt1.o" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../lib64/crti.o" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/crtbegin.o" "-L/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3" "-L/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../lib64" "-L/usr/bin/../lib64" "-L/lib/../lib64" "-L/usr/lib/../lib64" "-L/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3" "-L/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../.." "-L/usr/bin/../lib" "-L/lib" "-L/usr/lib" "/tmp/Hello-99daa5.o" "-lgcc" "--as-needed" "-lgcc_s" "--no-as-needed" "-lc" "-lgcc" "--as-needed" "-lgcc_s" "--no-as-needed" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/crtend.o" "/usr/bin/../lib/gcc/mips64el-redhat-linux/4.9.3/../../../../lib64/crtn.o"
***********************************************************************
The operation steps 4-9 are omitted here, but the execution results are correct.
***********************************************************************
#10. Simplify the above [4-9] stages
clang++ -save-temps Hello.cpp -o Hello
[root@localhost Hello]# clang++ -save-temps Hello.cpp -o Hello
[root@localhost Hello]# ./Hello
Hello World!In the clang 3.8.1 environment, the error reported by the C++ HelloWorld
program is maybe related to libstdc++. But the program compiled by clang8.0.0
can run normally, which makes me feel confused? Because during in two
compilation, I just updated the llvm+clang rpm packages to 8.0.0 version.
***************************************************************************
#1.compile method
[root@localhost Hello]# clang++ --save-temps -g -o Hello Hello.cpp
#2.Error info
[root@localhost Hello]# ./Hello
-bash: ./Hello: /lib64/ld-musl-mipsel.so.1: bad ELF interpreter: No such file
or directory
#3.Related links about above issue from google
(1)https://gist.github.com/mscdex/06e39ba86de0585e92ed
(2)https://git.realms.tech/JTRealms/lede-
wrt1900v1/commit/5ae9a4f830f369b4e8cf20d5bc569946f7cae06e
***************************************************************************Your teacher was right - bugs in standard libraries rarely happens. More often the problem is in the code which use/call libraries routines.
As to the "/lib64/ld-musl-mipsel.so.1: bad ELF interpreter: No such file or directory" error - Clang driver passes incorrect arguments to the linker "-dynamic-linker /lib64/ld-musl-mipsel.so.1". This is a bug in the Clang which has been fixed. That's why Clang 8 works ok.
I think you have to resolve problems in compilation your HelloWorld OpneCL example using Clang 8.0. This version of compiler has a lot of fixed bugs in comparison with the Clang 3.0. I'm not an expert in Mesa, but it looks like you need to update its version. The same problem described here https://bugs.freedesktop.org/show_bug.cgi?id=98627.
Quuxplusone
commented
5 years ago @Simon Atanasyan
Thank you very much for your tips. Now I have solved the problem of the HelloWorld (opencl program) program crash in the attachment.At the same time, when running C++ HelloWorld with clang 3.8.1 environment, the "ld-musl-mipsel.so.1" dynamic library can't be found, which can be solved by creating the following software link.
********************************************************************[loongson@localhost
Downloads]$ sudo ln -s /lib64/ld-2.20.so /lib64/ld-musl-mipsel.so.1
********************************************************************
Although the problem was solved in this way, I did not understand the mechanism. After many attempts, the last version of mesa I chose was mesa-18.0.5.
For the combination of clang 3.8.1 + mesa 11, if my work plan for the second half of the year goes well, I will do further research, but I don't know what it means? Can you give me some guidance? Should I give up this combination? Looking forward to your reply.
At this point, everything is going well, thank you again for your mention and guidance.
You can choose to turn off this bug or minimize its priority. Thanks.
HelloWorld.zip(3541 bytes, application/zip)