FreeBSD Bugzilla – Attachment 184402 Details for
Bug 220767
lang/beignet: hangs if consumer is not linked against libpthread after jemalloc 5.0.0 update
Home
|
New
|
Browse
|
Search
|
[?]
|
Reports
|
Help
|
New Account
|
Log In
Remember
[x]
|
Forgot Password
Login:
[x]
"bt full" output
bt-f.txt (text/plain), 11.70 KB, created by
Jan Beich
on 2017-07-16 15:26:18 UTC
(
hide
)
Description:
"bt full" output
Filename:
MIME Type:
Creator:
Jan Beich
Created:
2017-07-16 15:26:18 UTC
Size:
11.70 KB
patch
obsolete
>(gdb) bt f >#0 _umtx_op_err () at /usr/src/lib/libthr/arch/amd64/amd64/_umtx_op_err.S:37 >No locals. >#1 0x0000000803c579e4 in __thr_umutex_lock (mtx=0x803e7dc78 <_mutex_static_lock>, id=101914) > at /usr/src/lib/libthr/thread/thr_umtx.c:80 > owner = 101914 >#2 0x0000000803c61acc in _thr_umutex_lock (mtx=0x803e7dc78 <_mutex_static_lock>, id=101914) > at /usr/src/lib/libthr/thread/thr_umtx.h:123 >No locals. >#3 0x0000000803c619b4 in init_static (thread=0x80068b000, mutex=0x801348e50) > at /usr/src/lib/libthr/thread/thr_mutex.c:304 > ret = 8 >#4 0x0000000803c602f8 in check_and_init_mutex (mutex=0x801348e50, m=0x7fffffff2de0) > at /usr/src/lib/libthr/thread/thr_mutex.c:598 > ret = 0 >#5 0x0000000803c5f689 in __pthread_mutex_trylock (mutex=0x801348e50) > at /usr/src/lib/libthr/thread/thr_mutex.c:614 > curthread = 0x1cfffee378 > m = 0x0 > id = 32767 > ret = -53201 > robust = 1 >#6 0x0000000800d656b9 in malloc_mutex_trylock_final (mutex=0x801348e10) > at /usr/src/contrib/jemalloc/include/jemalloc/internal/mutex.h:144 >No locals. >#7 0x0000000800d59602 in malloc_mutex_lock (tsdn=0x80063c088, mutex=0x801348e10) > at /usr/src/contrib/jemalloc/include/jemalloc/internal/mutex.h:202 >No locals. >#8 0x0000000800d5b6b8 in __je_arena_tcache_fill_small (tsdn=0x80063c088, arena=0x801344980, > tcache=0x80063c240, tbin=0x80063c2e0, binind=6, prof_accumbytes=0) at jemalloc_arena.c:1433 > i = 8 > nfill = 6537352 > bin = 0x801348e10 >#9 0x0000000800cd7013 in __je_tcache_alloc_small_hard (tsdn=0x80063c088, arena=0x801344980, > tcache=0x80063c240, tbin=0x80063c2e0, binind=6, tcache_success=0x7fffffff53f6) > at jemalloc_tcache.c:93 > ret = 0x1cfffecd20 >#10 0x0000000800d8ea3e in tcache_alloc_small (tsd=0x80063c088, arena=0x801344980, > tcache=0x80063c240, size=96, binind=6, zero=true, slow_path=false) > at /usr/src/contrib/jemalloc/include/jemalloc/internal/tcache_inlines.h:86 > tcache_hard_success = false > ret = 0x0 > tbin = 0x80063c2e0 > tcache_success = false > usize = 0 >#11 arena_malloc (tsdn=0x80063c088, arena=0x0, size=96, ind=6, zero=true, tcache=0x80063c240, > slow_path=false) at /usr/src/contrib/jemalloc/include/jemalloc/internal/arena_inlines_b.h:101 >No locals. >#12 iallocztm (tsdn=0x80063c088, size=96, ind=6, zero=true, tcache=0x80063c240, is_internal=false, > arena=0x0, slow_path=false) > at /usr/src/contrib/jemalloc/include/jemalloc/internal/jemalloc_internal_inlines_c.h:33 > ret = 0x7fffffff4560 >#13 imalloc_no_sample (sopts=0x7fffffff5300, dopts=0x7fffffff52d0, tsd=0x80063c088, size=96, > usize=96, ind=6) at jemalloc_jemalloc.c:1654 > tcache = 0x80063c240 > arena = 0x0 >#14 imalloc_body (sopts=0x7fffffff5300, dopts=0x7fffffff52d0, tsd=0x80063c088) > at jemalloc_jemalloc.c:1850 > allocation = 0x0 > size = 96 > ind = 6 > usize = 96 > reentrancy_level = 0 '\000' >#15 imalloc (sopts=0x7fffffff5300, dopts=0x7fffffff52d0) at jemalloc_jemalloc.c:1950 > tsd = 0x80063c088 >#16 __calloc (num=1, size=96) at jemalloc_jemalloc.c:2064 > ret = 0x1 > sopts = {may_overflow = true, bump_empty_alloc = true, assert_nonempty_alloc = false, > null_out_result_on_error = true, set_errno_on_error = true, min_alignment = 0, > oom_string = 0x800ecf1d2 "<jemalloc>: Error in calloc(): out of memory\n", > invalid_alignment_string = 0x800ecd8ad "", slow = false} > dopts = {result = 0x7fffffff5328, num_items = 1, item_size = 96, alignment = 0, > zero = true, tcache_ind = 4294967294, arena_ind = 4294967295} >#17 0x0000000803c5fc0e in mutex_init (mutex=0x801348e50, > mutex_attr=0x803e72758 <_pthread_mutexattr_default>, calloc_cb=0x800d8bea0 <__calloc>) > at /usr/src/lib/libthr/thread/thr_mutex.c:292 > attr = 0x803e72758 <_pthread_mutexattr_default> > pmutex = 0x7fffffff6050 > error = 0 >#18 0x0000000803c619dc in init_static (thread=0x80068b000, mutex=0x801348e50) > at /usr/src/lib/libthr/thread/thr_mutex.c:307 > ret = 8 >#19 0x0000000803c602f8 in check_and_init_mutex (mutex=0x801348e50, m=0x7fffffff60d0) > at /usr/src/lib/libthr/thread/thr_mutex.c:598 > ret = 0 >#20 0x0000000803c5f689 in __pthread_mutex_trylock (mutex=0x801348e50) > at /usr/src/lib/libthr/thread/thr_mutex.c:614 > curthread = 0x80063c248 > m = 0x0 > id = 8 > ret = 14522970 > robust = 8 >#21 0x0000000800d656b9 in malloc_mutex_trylock_final (mutex=0x801348e10) > at /usr/src/contrib/jemalloc/include/jemalloc/internal/mutex.h:144 >No locals. >#22 0x0000000800d59602 in malloc_mutex_lock (tsdn=0x80063c088, mutex=0x801348e10) > at /usr/src/contrib/jemalloc/include/jemalloc/internal/mutex.h:202 >No locals. >#23 0x0000000800d5b6b8 in __je_arena_tcache_fill_small (tsdn=0x80063c088, arena=0x801344980, > tcache=0x80063c240, tbin=0x80063c2e0, binind=6, prof_accumbytes=0) at jemalloc_arena.c:1433 > i = 8 > nfill = 6537352 > bin = 0x801348e10 >#24 0x0000000800cd7013 in __je_tcache_alloc_small_hard (tsdn=0x80063c088, arena=0x801344980, > tcache=0x80063c240, tbin=0x80063c2e0, binind=6, tcache_success=0x7fffffff86d6) > at jemalloc_tcache.c:93 > ret = 0x80063c088 >#25 0x0000000800d72886 in tcache_alloc_small (tsd=0x80063c088, arena=0x801344980, > tcache=0x80063c240, size=88, binind=6, zero=false, slow_path=false) > at /usr/src/contrib/jemalloc/include/jemalloc/internal/tcache_inlines.h:86 > tcache_hard_success = false > ret = 0x0 > tbin = 0x80063c2e0 > tcache_success = false > usize = 0 >#26 arena_malloc (tsdn=0x80063c088, arena=0x0, size=88, ind=6, zero=false, tcache=0x80063c240, > slow_path=false) at /usr/src/contrib/jemalloc/include/jemalloc/internal/arena_inlines_b.h:101 >No locals. >#27 iallocztm (tsdn=0x80063c088, size=88, ind=6, zero=false, tcache=0x80063c240, is_internal=false, > arena=0x0, slow_path=false) > at /usr/src/contrib/jemalloc/include/jemalloc/internal/jemalloc_internal_inlines_c.h:33 > ret = 0x20 >#28 imalloc_no_sample (sopts=0x7fffffff85e0, dopts=0x7fffffff85b0, tsd=0x80063c088, size=88, > usize=96, ind=6) at jemalloc_jemalloc.c:1654 > tcache = 0x80063c240 > arena = 0x0 >#29 imalloc_body (sopts=0x7fffffff85e0, dopts=0x7fffffff85b0, tsd=0x80063c088) > at jemalloc_jemalloc.c:1850 > allocation = 0x0 > size = 88 > ind = 6 > usize = 96 > reentrancy_level = 0 '\000' >#30 imalloc (sopts=0x7fffffff85e0, dopts=0x7fffffff85b0) at jemalloc_jemalloc.c:1950 > tsd = 0x80063c088 >#31 __malloc (size=88) at jemalloc_jemalloc.c:1981 > ret = 0x8ffffffff > sopts = {may_overflow = false, bump_empty_alloc = true, assert_nonempty_alloc = false, > null_out_result_on_error = true, set_errno_on_error = true, min_alignment = 0, > oom_string = 0x800ecf128 "<jemalloc>: Error in malloc(): out of memory\n", > invalid_alignment_string = 0x800ecd8ad "", slow = false} > dopts = {result = 0x7fffffff8608, num_items = 1, item_size = 88, alignment = 0, > zero = false, tcache_ind = 4294967294, arena_ind = 4294967295} >#32 0x00000008033b81a8 in operator new (size=88) at /usr/src/contrib/libc++/src/new.cpp:70 > p = 0x808fc93e0 >#33 0x000000080803aa89 in llvm::User::operator new(unsigned long, unsigned int) () > from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#34 0x0000000806ea6b34 in clang::CodeGen::CodeGenFunction::StartFunction(clang::GlobalDecl, clang::QualType, llvm::Function*, clang::CodeGen::CGFunctionInfo const&, clang::CodeGen::FunctionArgList const&, clang::SourceLocation, clang::SourceLocation) () from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#35 0x0000000806ea8551 in clang::CodeGen::CodeGenFunction::GenerateCode(clang::GlobalDecl, llvm::Function*, clang::CodeGen::CGFunctionInfo const&) () from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#36 0x0000000806eba8d9 in clang::CodeGen::CodeGenModule::EmitGlobalFunctionDefinition(clang::GlobalDecl, llvm::GlobalValue*) () from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#37 0x0000000806eb6774 in clang::CodeGen::CodeGenModule::EmitGlobalDefinition(clang::GlobalDecl, llvm::GlobalValue*) () from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#38 0x0000000806ebc322 in clang::CodeGen::CodeGenModule::EmitTopLevelDecl(clang::Decl*) () > from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#39 0x0000000806e3c82f in (anonymous namespace)::CodeGeneratorImpl::HandleTopLevelDecl(clang::DeclGroupRef) () from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#40 0x0000000806e2fb85 in clang::BackendConsumer::HandleTopLevelDecl(clang::DeclGroupRef) () > from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#41 0x00000008077d0462 in clang::ParseAST(clang::Sema&, bool, bool) () > from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#42 0x0000000806bdc2b9 in clang::FrontendAction::Execute() () from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#43 0x0000000806ba2cf1 in clang::CompilerInstance::ExecuteAction(clang::FrontendAction&) () > from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >basic_string<char, std::__1::char_traits<char>, std::__1::allocator<char> >, std::__1::allocator<std::__1::basic_string<char, std::__1::char_traits<char>, std::__1::allocator<char> > > >&, unsigned long, char*, unsigned long*, unsigned int) () from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#45 0x00000008067848b3 in gbe::programNewFromSource(unsigned int, char const*, unsigned long, char const*, char*, unsigned long*) () from /usr/local/lib/beignet//libgbe.so >No symbol table info available. >#46 0x00000008019617c7 in cl_program_build (p=0x8006cd1c0, options=0x801992f4d "") > at src/cl_program.c:626 > err = 0 > i = 0 > copyed = 0 > ocl_version = 0 >#47 0x0000000801952782 in clBuildProgram (program=0x8006cd1c0, num_devices=1, > device_list=0x7fffffffe050, options=0x801992f4d "", pfn_notify=0x0, user_data=0x0) > at src/cl_api.c:835 > err = 0 >#48 0x00000008019757b4 in cl_self_test (device=0x801bcf2a0 <intel_skl_gt2_device>, > atomic_in_l3_flag=SELF_TEST_PASS) at src/cl_device_id.c:856 > tested = 1 > ret = SELF_TEST_OTHER_FAIL > status = 0 > ctx = 0x80068e700 > queue = 0x8006c5240 > program = 0x8006cd1c0 > kernel = 0x43e046000 > buffer = 0x8 > kernel_finished = 0x80000000 > n = 3 > test_data = {3, 7, 5} > kernel_source = 0x801991f84 "__kernel void self_test(__global int *buf) { __local int tmp[3]; tmp[get_local_id(0)] = buf[get_local_id(0)]; barrier(CLK_LOCAL_MEM_FENCE); buf[get_global_id(0)] = tmp[2 - get_local_id(0)] + buf[g"... >#49 0x0000000801975a3e in cl_get_device_ids (platform=0x801bcb3d8 <intel_platform_data>, > device_type=4294967295, num_entries=0, devices=0x0, num_devices=0x8007e8cf0) > at src/cl_device_id.c:911 > ret = 8 > device = 0x801bcf2a0 <intel_skl_gt2_device> >#50 0x00000008019554b3 in clGetDeviceIDs (platform=0x801bcb3d8 <intel_platform_data>, > device_type=4294967295, num_entries=0, devices=0x0, num_devices=0x8007e8cf0) > at src/cl_api_device_id.c:43 > valid_type = 31 >#51 0x000000080083e065 in clGetDeviceIDs (platform=0x801bcb3d8 <intel_platform_data>, > device_type=4294967295, num_entries=0, devices=0x0, num_devices=0x8007e8cf0) > at ocl_icd_loader_gen.c:58 > ret = -1 >#52 0x0000000000402341 in printPlatformInfo (p=0) at src/clinfo.c:459 > pid = 0x801bcb3d8 <intel_platform_data> > len = 5 > pinfo_checks = {has_khr_icd = 1, plat_version = 20} >#53 0x000000000040a3bd in main (argc=1, argv=0x7fffffffe2b8) at src/clinfo.c:2676 > p = 0 > a = 1 > show_offline = 0
You cannot view the attachment while viewing its details because your browser does not support IFRAMEs.
View the attachment on a separate page
.
View Attachment As Raw
Actions:
View
Attachments on
bug 220767
: 184402