public inbox for gcc-bugs@sourceware.org
help / color / mirror / Atom feed
* [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl
@ 2013-10-06 13:42 vincenzo.innocente at cern dot ch
2013-10-06 13:56 ` [Bug libgomp/58642] " jakub at gcc dot gnu.org
` (26 more replies)
0 siblings, 27 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-06 13:42 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
Bug ID: 58642
Summary: gomp regression: not "honoring" anymore task set and
numactl
Product: gcc
Version: 4.9.0
Status: UNCONFIRMED
Severity: normal
Priority: P3
Component: libgomp
Assignee: unassigned at gcc dot gnu.org
Reporter: vincenzo.innocente at cern dot ch
CC: jakub at gcc dot gnu.org
till
[gomp-4_0-branch revision 202766]
int main() {
std::cout << "max thread "<< omp_get_max_threads() << std::endl;
}
taskset -c 0-3 ./a.out
max thread 4
now [gomp-4_0-branch revision 203223]
taskset -c 0-3 ./a.out
max thread 32
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
@ 2013-10-06 13:56 ` jakub at gcc dot gnu.org
2013-10-06 14:05 ` jakub at gcc dot gnu.org
` (25 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-06 13:56 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #1 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
Weird, can't reproduce.
/tmp/ttt
8
taskset -c 0-3 /tmp/ttt
4
ldd /tmp/ttt | grep libgomp
libgomp.so.1 =>
/usr/src/gomp-4.0/obj/x86_64-unknown-linux-gnu/libgomp/.libs/libgomp.so.1
(0x00007fda5e2e8000)
strace /tmp/ttt 2>&1 | grep affinity
sched_getaffinity(30384, 8, {ff}) = 8
taskset -c 0-3 strace /tmp/ttt 2>&1 | grep affinity
sched_getaffinity(30389, 8, {f}) = 8
Do you have the default linux build (i.e. --enable-linux-futex), or one without
that (that doesn't honor affinity)?
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
2013-10-06 13:56 ` [Bug libgomp/58642] " jakub at gcc dot gnu.org
@ 2013-10-06 14:05 ` jakub at gcc dot gnu.org
2013-10-06 14:38 ` vincenzo.innocente at cern dot ch
` (24 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-06 14:05 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #2 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
What exact glibc do you use? I think the earliest that supports affinity in
libgomp should be 2.3, then between that and 2.7 there were multiple header
changes that the code just attempts to deal with using #ifdefs and finally 2.7
and newer should have the same headers as current glibc from what libgomp
needs.
I admit I have only tested it with glibc 2.17.
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
2013-10-06 13:56 ` [Bug libgomp/58642] " jakub at gcc dot gnu.org
2013-10-06 14:05 ` jakub at gcc dot gnu.org
@ 2013-10-06 14:38 ` vincenzo.innocente at cern dot ch
2013-10-06 15:15 ` vincenzo.innocente at cern dot ch
` (23 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-06 14:38 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #3 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
strange indeed
rhel6: so is 2.12
or my own version
GNU C Library stable release version 2.13,
I build gcc by myself
c++ -v
Using built-in specs.
COLLECT_GCC=c++
COLLECT_LTO_WRAPPER=/afs/cern.ch/user/i/innocent/w2/libexec/gcc/x86_64-unknown-linux-gnu/4.9.0/lto-wrapper
Target: x86_64-unknown-linux-gnu
Configured with: ../gcc-gomp4/configure
--prefix=/afs/cern.ch/user/i/innocent/w2 --enable-languages=c,c++,lto,fortran
-enable-gold=yes --enable-lto --with-build-config=bootstrap-lto
--with-gmp-lib=/usr/local/lib64 --with-mpfr-lib=/usr/local/lib64
-with-mpc-lib=/usr/local/lib64 --enable-cloog-backend=isl
--with-cloog=/usr/local --with-ppl-lib=/usr/local/lib64 CFLAGS='-O2
-ftree-vectorize -fPIC' -enable-libitm -disable-multilib -disable-werror
--disable-libsanitizer
same since long time
behavior changed yestarday when finally got gomp4 compiling…
I get
on one machine
uname -a
Linux vinavx0.cern.ch 2.6.32-358.18.1.el6.x86_64 #1 SMP Wed Aug 28 09:02:47
CEST 2013 x86_64 x86_64 x86_64 GNU/Linux
innocent@vinavx0 parallel]$ taskset -c 0-3 strace ./a.out | & grep affinity
sched_getaffinity(17895, 8, { f }) = 8
sched_getaffinity(17895, 128, { f, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0
}) = 128
sched_setaffinity(17895, 8, { 1 }) = 0
[innocent@vinavx0 parallel]$ taskset -c 0-7 strace ./a.out | & grep affinity
sched_getaffinity(17898, 8, { ff }) = 8
sched_getaffinity(17898, 128, { ff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0 }) = 128
sched_setaffinity(17898, 8, { 1 }) = 0
[innocent@vinavx0 parallel]$ taskset -c 0-3 ./a.out
max thread 4
[innocent@vinavx0 parallel]$ taskset -c 0-7 ./a.out
max thread 8
and indeed on this works
on the Xeon where I'm doing all tests (identical software stack: it's on shared
disks)
uname -a
Linux olsnba03 2.6.32-358.2.1.el6.x86_64 #1 SMP Wed Mar 13 08:24:06 CET 2013
x86_64 x86_64 x86_64 GNU/Linux
taskset -c 0-3 strace ./a.out | & grep affinity
sched_getaffinity(80664, 8, 0x1a69010) = -1 EINVAL (Invalid argument)
some with a different kernel
[innocent@olsnba04 parallel]$ uname -a
Linux olsnba04 3.10.2-1.el6.elrepo.x86_64 #1 SMP Mon Jul 22 12:18:13 EDT 2013
x86_64 x86_64 x86_64 GNU/Linux
[innocent@olsnba04 parallel]$ strace ./a.out | & grep affinity
sched_getaffinity(55293, 8, 0x225b010) = -1 EINVAL (Invalid argument)
[innocent@olsnba04 parallel]$ taskset -c 0-3 strace ./a.out | & grep affinity
sched_getaffinity(55297, 8, 0xbca010) = -1 EINVAL (Invalid argument)
[innocent@olsnba04 parallel]$
libgc always 2.13
on this very same machine tried the test program in man page
cat affTest.cpp
#define _GNU_SOURCE
#include <sched.h>
#include <stdio.h>
#include <errno.h>
int main(void)
{
cpu_set_t *mask;
size_t size;
int i;
int nrcpus = 1024;
realloc:
mask = CPU_ALLOC(nrcpus);
size = CPU_ALLOC_SIZE(nrcpus);
CPU_ZERO_S(size, mask);
if ( sched_getaffinity(0, size, mask) == -1 ) {
CPU_FREE(mask);
if (errno == EINVAL &&
nrcpus < (1024 << 8)) {
nrcpus = nrcpus << 2;
goto realloc;
}
perror("sched_getaffinity");
return -1;
}
for ( i = 0; i < nrcpus; i++ ) {
if ( CPU_ISSET_S(i, size, mask) ) {
printf("CPU %d is set\n", (i+1));
}
}
CPU_FREE(mask);
return 0;
}
gcc affTest.cpp
./a.out
CPU 1 is set
CPU 2 is set
CPU 3 is set
CPU 4 is set
CPU 5 is set
CPU 6 is set
CPU 7 is set
CPU 8 is set
CPU 9 is set
CPU 10 is set
CPU 11 is set
CPU 12 is set
CPU 13 is set
CPU 14 is set
CPU 15 is set
CPU 16 is set
CPU 17 is set
CPU 18 is set
CPU 19 is set
CPU 20 is set
CPU 21 is set
CPU 22 is set
CPU 23 is set
CPU 24 is set
CPU 25 is set
CPU 26 is set
CPU 27 is set
CPU 28 is set
CPU 29 is set
CPU 30 is set
CPU 31 is set
CPU 32 is set
[innocent@olsnba04 parallel]$ taskset -c 0-3 ./a.out
CPU 1 is set
CPU 2 is set
CPU 3 is set
CPU 4 is set
[innocent@olsnba04 parallel]$ taskset -c 0-3 strace ./a.out |& grep aff
sched_getaffinity(0, 128, { f, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0 })
= 128
[innocent@olsnba04 parallel]$ strace ./a.out | & grep aff
sched_getaffinity(0, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0 }) = 128
BUT
c++ -Ofast -fopenmp -std=c++11 affTest.cpp
affTest.cpp:1:0: warning: "_GNU_SOURCE" redefined [enabled by default]
#define _GNU_SOURCE
^
<command-line>:0:0: note: this is the location of the previous definition
[innocent@olsnba04 parallel]$ strace ./a.out | & grep aff
sched_getaffinity(55390, 8, 0x1709010) = -1 EINVAL (Invalid argument)
sched_getaffinity(0, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0 }) = 128
>From gcc-bugs-return-431187-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org Sun Oct 06 14:43:13 2013
Return-Path: <gcc-bugs-return-431187-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org>
Delivered-To: listarch-gcc-bugs@gcc.gnu.org
Received: (qmail 5566 invoked by alias); 6 Oct 2013 14:43:13 -0000
Mailing-List: contact gcc-bugs-help@gcc.gnu.org; run by ezmlm
Precedence: bulk
List-Id: <gcc-bugs.gcc.gnu.org>
List-Archive: <http://gcc.gnu.org/ml/gcc-bugs/>
List-Post: <mailto:gcc-bugs@gcc.gnu.org>
List-Help: <mailto:gcc-bugs-help@gcc.gnu.org>
Sender: gcc-bugs-owner@gcc.gnu.org
Delivered-To: mailing list gcc-bugs@gcc.gnu.org
Received: (qmail 5521 invoked by uid 55); 6 Oct 2013 14:43:10 -0000
From: "paolo at gcc dot gnu.org" <gcc-bugzilla@gcc.gnu.org>
To: gcc-bugs@gcc.gnu.org
Subject: [Bug c++/56060] ICE on invalid code in type_dependent_expression_p, at cp/pt.c:19742
Date: Sun, 06 Oct 2013 14:43:00 -0000
X-Bugzilla-Reason: CC
X-Bugzilla-Type: changed
X-Bugzilla-Watch-Reason: None
X-Bugzilla-Product: gcc
X-Bugzilla-Component: c++
X-Bugzilla-Version: 4.8.0
X-Bugzilla-Keywords: ice-on-invalid-code
X-Bugzilla-Severity: minor
X-Bugzilla-Who: paolo at gcc dot gnu.org
X-Bugzilla-Status: ASSIGNED
X-Bugzilla-Priority: P3
X-Bugzilla-Assigned-To: paolo.carlini at oracle dot com
X-Bugzilla-Target-Milestone: 4.9.0
X-Bugzilla-Flags:
X-Bugzilla-Changed-Fields:
Message-ID: <bug-56060-4-tKXvqtb8Hl@http.gcc.gnu.org/bugzilla/>
In-Reply-To: <bug-56060-4@http.gcc.gnu.org/bugzilla/>
References: <bug-56060-4@http.gcc.gnu.org/bugzilla/>
Content-Type: text/plain; charset="UTF-8"
Content-Transfer-Encoding: 7bit
X-Bugzilla-URL: http://gcc.gnu.org/bugzilla/
Auto-Submitted: auto-generated
MIME-Version: 1.0
X-SW-Source: 2013-10/txt/msg00331.txt.bz2
Content-length: 682
http://gcc.gnu.org/bugzilla/show_bug.cgi?idV060
--- Comment #4 from paolo at gcc dot gnu.org <paolo at gcc dot gnu.org> ---
Author: paolo
Date: Sun Oct 6 14:43:07 2013
New Revision: 203229
URL: http://gcc.gnu.org/viewcvs?rev 3229&root=gcc&view=rev
Log:
/cp
2013-10-06 Paolo Carlini <paolo.carlini@oracle.com>
PR c++/56060
* pt.c (type_dependent_expression_p): Handle EXPR_PACK_EXPANSION.
/testsuite
2013-10-06 Paolo Carlini <paolo.carlini@oracle.com>
PR c++/56060
* g++.dg/cpp0x/variadic144.C: New.
Added:
trunk/gcc/testsuite/g++.dg/cpp0x/variadic144.C
Modified:
trunk/gcc/cp/ChangeLog
trunk/gcc/cp/pt.c
trunk/gcc/testsuite/ChangeLog
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (2 preceding siblings ...)
2013-10-06 14:38 ` vincenzo.innocente at cern dot ch
@ 2013-10-06 15:15 ` vincenzo.innocente at cern dot ch
2013-10-06 18:02 ` jakub at gcc dot gnu.org
` (22 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-06 15:15 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #4 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
24 thread machine ok
innocent@vocms19 parallel]$ c++ -Ofast -std=c++11 -fopenmp simpleOMP.cpp
[innocent@vocms19 parallel]$ ./a.out
max thread 24
[innocent@vocms19 parallel]$ taskset -c 0-3 ./a.out
max thread 4
strace ./a.out | & grep affi
sched_getaffinity(9720, 8, { ffffff }) = 8
[innocent@vocms19 parallel]$ taskset -c 0-3 strace ./a.out | & grep affi
sched_getaffinity(9723, 8, { f }) = 8
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (3 preceding siblings ...)
2013-10-06 15:15 ` vincenzo.innocente at cern dot ch
@ 2013-10-06 18:02 ` jakub at gcc dot gnu.org
2013-10-06 19:31 ` jakub at gcc dot gnu.org
` (21 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-06 18:02 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #5 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
So, looking at kernel sources, it seems it returns EINVAL:
if ((len * BITS_PER_BYTE) < nr_cpu_ids)
return -EINVAL;
so the question is how to find what your nr_cpu_ids is and how to (cheaply)
query it from userland.
I was using sysconf (_SC_NPROCESSORS_CONF) for that, which is what I saw when
googling around for what upper bound to pass to pthread_getaffinity_np when I
want to dynamically support more than 1024 CPUs, but thought it would work fine
to pass just CPU_ALLOC_SIZE of the sysconf return value.
What do you get from
getconf -a | grep _NPROCESSORS
? What is the minimum cpusetsize that pthread_getaffinity_np doesn't fail
with?
ls -l /sys/devices/system/cpu/
? I'd strongly prefer not to use say minimum of CPU_ALLOC_SIZE (sysconf
(_SC_NPROCESSORS_CONF)) and CPUSETSIZE, I need cpusetsize sized bitmap for
every place in the OMP_PLACES list (or every thread, core resp. socket), so
having to allocate 128 bytes per each rather than say 8 on <= 64 CPU box sounds
overkill to me.
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (4 preceding siblings ...)
2013-10-06 18:02 ` jakub at gcc dot gnu.org
@ 2013-10-06 19:31 ` jakub at gcc dot gnu.org
2013-10-07 6:49 ` vincenzo.innocente at cern dot ch
` (20 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-06 19:31 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #6 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
Also, can you dmesg | grep 'Allowing.*CPUs'
(or grep /var/log/messages* for the same)?
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (5 preceding siblings ...)
2013-10-06 19:31 ` jakub at gcc dot gnu.org
@ 2013-10-07 6:49 ` vincenzo.innocente at cern dot ch
2013-10-07 6:53 ` vincenzo.innocente at cern dot ch
` (19 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 6:49 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #7 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
getconf -a | grep _NPROCESSORS
_NPROCESSORS_CONF 32
_NPROCESSORS_ONLN 32
ls -l /sys/devices/system/cpu/
total 0
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu0
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu1
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu10
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu11
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu12
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu13
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu14
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu15
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu16
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu17
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu18
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu19
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu2
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu20
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu21
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu22
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu23
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu24
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu25
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu26
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu27
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu28
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu29
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu3
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu30
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu31
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu4
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu5
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu6
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu7
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu8
drwxr-xr-x 8 root root 0 Sep 2 17:44 cpu9
drwxr-xr-x 2 root root 0 Sep 2 17:45 cpufreq
drwxr-xr-x 2 root root 0 Sep 2 17:45 cpuidle
drwxr-xr-x 2 root root 0 Oct 7 08:43 intel_pstate
-r--r--r-- 1 root root 4096 Oct 7 08:43 kernel_max
-r--r--r-- 1 root root 4096 Oct 7 08:43 modalias
-r--r--r-- 1 root root 4096 Oct 7 08:43 offline
-r--r--r-- 1 root root 4096 Sep 2 18:06 online
-r--r--r-- 1 root root 4096 Oct 7 08:43 possible
drwxr-xr-x 2 root root 0 Oct 7 08:43 power
-r--r--r-- 1 root root 4096 Oct 7 08:43 present
--w------- 1 root root 4096 Oct 7 08:43 probe
--w------- 1 root root 4096 Oct 7 08:43 release
-rw-r--r-- 1 root root 4096 Oct 7 08:43 uevent
dmesg | grep 'Allowing.*CPUs'
smpboot: Allowing 128 CPUs, 96 hotplug CPUs
#include <sched.h>
#include <stdio.h>
#include <errno.h>
int main(void)
{
cpu_set_t k[32];
sched_getaffinity(0, 8, k);
sched_getaffinity(0, 10, k);
sched_getaffinity(0, 12, k);
sched_getaffinity(0, 16, k);
strace ./a.out |& grep affin
sched_getaffinity(0, 8, 0x7fffbcf19420) = -1 EINVAL (Invalid argument)
sched_getaffinity(0, 10, 0x7fffbcf19420) = -1 EINVAL (Invalid argument)
sched_getaffinity(0, 12, 0x7fffbcf19420) = -1 EINVAL (Invalid argument)
sched_getaffinity(0, 16, { ffffffff, 0 }) = 16
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (6 preceding siblings ...)
2013-10-07 6:49 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 6:53 ` vincenzo.innocente at cern dot ch
2013-10-07 7:47 ` jakub at gcc dot gnu.org
` (18 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 6:53 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #8 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
do you have access to a >32 cpu machine?
btw on XEON-PHI one can have >200 "cpus"
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (7 preceding siblings ...)
2013-10-07 6:53 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 7:47 ` jakub at gcc dot gnu.org
2013-10-07 7:58 ` vincenzo.innocente at cern dot ch
` (17 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-07 7:47 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
Jakub Jelinek <jakub at gcc dot gnu.org> changed:
What |Removed |Added
----------------------------------------------------------------------------
Status|UNCONFIRMED |ASSIGNED
Last reconfirmed| |2013-10-07
Assignee|unassigned at gcc dot gnu.org |jakub at gcc dot gnu.org
Ever confirmed|0 |1
--- Comment #9 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
Created attachment 30964
--> http://gcc.gnu.org/bugzilla/attachment.cgi?id=30964&action=edit
gomp-pr58642.patch
Can you please try this patch? From the above it seems there is no easy way to
find out what is the minimum size to make pthread_getaffinity_np pass, on the
other side it should be fine to pass smaller size to pthread_setaffinity_np.
So, what the patch tries to do is if the initial pthread_getaffinity_np failed
with EINVAL, it will retry with larger sizes, and, once it succeeds, tries to
find out the required minimum size that covers all the currently available
CPUs.
The minimum size for successful pthread_getaffinity_np will then be used for
further pthread_getaffinity_np calls, while gomp_cpuset_size will be used for
the places bitmasks and pthread_setaffinity_np calls.
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (8 preceding siblings ...)
2013-10-07 7:47 ` jakub at gcc dot gnu.org
@ 2013-10-07 7:58 ` vincenzo.innocente at cern dot ch
2013-10-07 8:04 ` jakub at gcc dot gnu.org
` (16 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 7:58 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #10 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
seems working
[innocent@olsnba04 parallel]$ c++ -std=c++11 -Ofast -fopenmp simpleOMP.cpp
[innocent@olsnba04 parallel]$ ./a.out
max thread 32
[innocent@olsnba04 parallel]$ taskset -c 0-3 ./a.out
max thread 4
[innocent@olsnba04 parallel]$ taskset -c 0-3 strace ./a.out |& grep aff
sched_getaffinity(72698, 8, 0x855010) = -1 EINVAL (Invalid argument)
sched_getaffinity(72698, 128, { f, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0
}) = 128
[innocent@olsnba04 parallel]$ taskset -c 0-15 strace ./a.out | & grep aff
sched_getaffinity(72702, 8, 0x1b2e010) = -1 EINVAL (Invalid argument)
sched_getaffinity(72702, 128, { ffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0 }) = 128
[innocent@olsnba04 parallel]$ strace ./a.out | & grep aff
sched_getaffinity(72705, 8, 0x25ff010) = -1 EINVAL (Invalid argument)
sched_getaffinity(72705, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (9 preceding siblings ...)
2013-10-07 7:58 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 8:04 ` jakub at gcc dot gnu.org
2013-10-07 8:06 ` jakub at gcc dot gnu.org
` (15 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-07 8:04 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #11 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
(In reply to vincenzo Innocente from comment #10)
> seems working
Thanks. Can you please also try some simple (with -fopenmp):
int
main (void)
{
#pragma omp parallel num_threads (32)
asm volatile ("" : : : "memory");
return 0;
}
with OMP_PROC_BIND=true and OMP_PLACES='threads'
(resp. cores resp. sockets resp. say {0:4}:4:8)
and post the strace -f sched_[sg]etaffinity syscalls from that?
I'd like to see whether it managed to properly use just size 8 for the
setaffinity syscalls, while 128 for getaffinity.
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (10 preceding siblings ...)
2013-10-07 8:04 ` jakub at gcc dot gnu.org
@ 2013-10-07 8:06 ` jakub at gcc dot gnu.org
2013-10-07 8:08 ` vincenzo.innocente at cern dot ch
` (14 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-07 8:06 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #12 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
Ah, and can you also do make check RUNTESTFLAGS=c.exp=affinity-1.c
in the libgomp build directory and see whether it was PASS and, if
testsuite/libgomp.log contains any lines ending with verified and none matching
'expected.*instead' regexp?
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (11 preceding siblings ...)
2013-10-07 8:06 ` jakub at gcc dot gnu.org
@ 2013-10-07 8:08 ` vincenzo.innocente at cern dot ch
2013-10-07 8:12 ` vincenzo.innocente at cern dot ch
` (13 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 8:08 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #13 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
[innocent@olsnba04 parallel]$ setenv OMP_PROC_BIND true; setenv OMP_PLACES
'threads'
[innocent@olsnba04 parallel]$ gcc -fopenmp trivialOMP.cpp
[innocent@olsnba04 parallel]$ ./a.out
[innocent@olsnba04 parallel]$ stace ./a.out |& grep aff
[innocent@olsnba04 parallel]$ strace ./a.out | & grep aff
sched_getaffinity(72881, 8, 0xc5c010) = -1 EINVAL (Invalid argument)
sched_getaffinity(72881, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
sched_getaffinity(72881, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
sched_setaffinity(72881, 8, { 1 }) = 0
sched_setaffinity(72882, 8, { 2 }) = 0
sched_setaffinity(72883, 8, { 4 }) = 0
sched_setaffinity(72884, 8, { 8 }) = 0
sched_setaffinity(72885, 8, { 10 }) = 0
sched_setaffinity(72886, 8, { 20 }) = 0
sched_setaffinity(72887, 8, { 40 }) = 0
mmap(NULL, 8392704, PROT_READ|PROT_WRITE, MAP_PRIVATE|MAP_ANONYMOUS|MAP_STACK,
-1, 0) = 0x7f5e9aff5000
mprotect(0x7f5e9aff5000, 4096, PROT_NONE) = 0
sched_setaffinity(72888, 8, { 80 }) = 0
clone(child_stack=0x7f5e9aff3f90,
flags=CLONE_VM|CLONE_FS|CLONE_FILES|CLONE_SIGHAND|CLONE_THREAD|CLONE_SYSVSEM|CLONE_SETTLS|CLONE_PARENT_SETTID|CLONE_CHILD_CLEARTID|CLONE_DETACHED,
parent_tidptr=0x7f5e9aff49d0, tls=0x7f5e9aff4700, child_tidptr=0x7f5e9aff49d0)
= 72889
sched_setaffinity(72889, 8, { 100 }) = 0
futex(0x7f5e9aff4d18, FUTEX_WAKE_PRIVATE, 1) = 1
sched_setaffinity(72890, 8, { 200 }) = 0
sched_setaffinity(72891, 8, { 400 }) = 0
sched_setaffinity(72892, 8, { 800 }) = 0
sched_setaffinity(72893, 8, { 1000 }) = 0
sched_setaffinity(72894, 8, { 2000 }) = 0
sched_setaffinity(72895, 8, { 4000 }) = 0
sched_setaffinity(72896, 8, { 8000 }) = 0
sched_setaffinity(72897, 8, { 10000 }) = 0
sched_setaffinity(72898, 8, { 20000 }) = 0
sched_setaffinity(72899, 8, { 40000 }) = 0
sched_setaffinity(72900, 8, { 80000 }) = 0
sched_setaffinity(72901, 8, { 100000 }) = 0
sched_setaffinity(72902, 8, { 200000 }) = 0
sched_setaffinity(72903, 8, { 400000 }) = 0
sched_setaffinity(72904, 8, { 800000 }) = 0
sched_setaffinity(72905, 8, { 1000000 }) = 0
sched_setaffinity(72906, 8, { 2000000 }) = 0
sched_setaffinity(72907, 8, { 4000000 }) = 0
sched_setaffinity(72908, 8, { 8000000 }) = 0
sched_setaffinity(72909, 8, { 10000000 }) = 0
sched_setaffinity(72910, 8, { 20000000 }) = 0
sched_setaffinity(72911, 8, { 40000000 }) = 0
sched_setaffinity(72912, 8, { 80000000 }) = 0
[innocent@olsnba04 parallel]$ strace -f ./a.out | & grep aff
sched_getaffinity(72917, 8, 0x1bd8010) = -1 EINVAL (Invalid argument)
sched_getaffinity(72917, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
sched_getaffinity(72917, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
sched_setaffinity(72917, 8, { 1 }) = 0
[pid 72917] sched_setaffinity(72918, 8, { 2 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72919, 8, { 4 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72920, 8, { 8 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72921, 8, { 10 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72922, 8, { 20 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72923, 8, { 40 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72924, 8, { 80 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72925, 8, { 100 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72926, 8, { 200 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72927, 8, { 400 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72928, 8, { 800 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72929, 8, { 1000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72930, 8, { 2000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72931, 8, { 4000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72932, 8, { 8000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72933, 8, { 10000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72934, 8, { 20000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72935, 8, { 40000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72936, 8, { 80000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72937, 8, { 100000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72938, 8, { 200000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72939, 8, { 400000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72940, 8, { 800000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72941, 8, { 1000000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72942, 8, { 2000000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72943, 8, { 4000000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72944, 8, { 8000000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72945, 8, { 10000000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72946, 8, { 20000000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72947, 8, { 40000000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
[pid 72917] sched_setaffinity(72948, 8, { 80000000 } <unfinished ...>
[pid 72917] <... sched_setaffinity resumed> ) = 0
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (12 preceding siblings ...)
2013-10-07 8:08 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 8:12 ` vincenzo.innocente at cern dot ch
2013-10-07 10:14 ` vincenzo.innocente at cern dot ch
` (12 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 8:12 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #14 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
On 7 Oct, 2013, at 10:06 AM, jakub at gcc dot gnu.org
<gcc-bugzilla@gcc.gnu.org> wrote:
> http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
>
> --- Comment #12 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
> Ah, and can you also do make check RUNTESTFLAGS=c.exp=affinity-1.c
> in the libgomp build directory and see whether it was PASS and, if
> testsuite/libgomp.log contains any lines ending with verified and none matching
> 'expected.*instead' regexp?
>
for "historical reason" I build gcc on my local workstation not on the XEON.
Also I do not have the gcc test infrastructure…
can I copy any of those test on the 32 cpu machine and run it locally?
v.
>
>From gcc-bugs-return-431232-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org Mon Oct 07 08:18:53 2013
Return-Path: <gcc-bugs-return-431232-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org>
Delivered-To: listarch-gcc-bugs@gcc.gnu.org
Received: (qmail 8891 invoked by alias); 7 Oct 2013 08:18:52 -0000
Mailing-List: contact gcc-bugs-help@gcc.gnu.org; run by ezmlm
Precedence: bulk
List-Id: <gcc-bugs.gcc.gnu.org>
List-Archive: <http://gcc.gnu.org/ml/gcc-bugs/>
List-Post: <mailto:gcc-bugs@gcc.gnu.org>
List-Help: <mailto:gcc-bugs-help@gcc.gnu.org>
Sender: gcc-bugs-owner@gcc.gnu.org
Delivered-To: mailing list gcc-bugs@gcc.gnu.org
Received: (qmail 8632 invoked by uid 48); 7 Oct 2013 08:18:48 -0000
From: "jakub at gcc dot gnu.org" <gcc-bugzilla@gcc.gnu.org>
To: gcc-bugs@gcc.gnu.org
Subject: [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
Date: Mon, 07 Oct 2013 08:18:00 -0000
X-Bugzilla-Reason: CC
X-Bugzilla-Type: changed
X-Bugzilla-Watch-Reason: None
X-Bugzilla-Product: gcc
X-Bugzilla-Component: libgomp
X-Bugzilla-Version: 4.9.0
X-Bugzilla-Keywords:
X-Bugzilla-Severity: normal
X-Bugzilla-Who: jakub at gcc dot gnu.org
X-Bugzilla-Status: ASSIGNED
X-Bugzilla-Priority: P3
X-Bugzilla-Assigned-To: jakub at gcc dot gnu.org
X-Bugzilla-Target-Milestone: ---
X-Bugzilla-Flags:
X-Bugzilla-Changed-Fields:
Message-ID: <bug-58642-4-MyKegPGDhD@http.gcc.gnu.org/bugzilla/>
In-Reply-To: <bug-58642-4@http.gcc.gnu.org/bugzilla/>
References: <bug-58642-4@http.gcc.gnu.org/bugzilla/>
Content-Type: text/plain; charset="UTF-8"
Content-Transfer-Encoding: quoted-printable
X-Bugzilla-URL: http://gcc.gnu.org/bugzilla/
Auto-Submitted: auto-generated
MIME-Version: 1.0
X-SW-Source: 2013-10/txt/msg00376.txt.bz2
Content-length: 718
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #15 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
(In reply to vincenzo Innocente from comment #14)
> for "historical reason" I build gcc on my local workstation not on the XEON.
> Also I do not have the gcc test infrastructure…
>
> can I copy any of those test on the 32 cpu machine and run it locally?
Sure, do make check RUNTESTFLAGS=c.exp=affinity-1.c
on your build box then, then cd testsuite/
grep affinity-1.exe libgomp.log
and copy the gcc command line to compile/link it, paste into shell, scp
affinity-1.exe to your 32way box, and run with
OMP_PROC_BIND=false ./affinity-1.exp
(against the new libgomp.so.1 of course).
>From gcc-bugs-return-431234-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org Mon Oct 07 08:32:59 2013
Return-Path: <gcc-bugs-return-431234-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org>
Delivered-To: listarch-gcc-bugs@gcc.gnu.org
Received: (qmail 21525 invoked by alias); 7 Oct 2013 08:32:58 -0000
Mailing-List: contact gcc-bugs-help@gcc.gnu.org; run by ezmlm
Precedence: bulk
List-Id: <gcc-bugs.gcc.gnu.org>
List-Archive: <http://gcc.gnu.org/ml/gcc-bugs/>
List-Post: <mailto:gcc-bugs@gcc.gnu.org>
List-Help: <mailto:gcc-bugs-help@gcc.gnu.org>
Sender: gcc-bugs-owner@gcc.gnu.org
Delivered-To: mailing list gcc-bugs@gcc.gnu.org
Received: (qmail 21118 invoked by uid 48); 7 Oct 2013 08:32:55 -0000
From: "mpolacek at gcc dot gnu.org" <gcc-bugzilla@gcc.gnu.org>
To: gcc-bugs@gcc.gnu.org
Subject: [Bug tree-optimization/58653] [4.7/4.8/4.9 Regression] wrong code (segfaults) at -O3 on x86_64-linux-gnu in 64-bit mode (affecting gcc 4.6 to trunk)
Date: Mon, 07 Oct 2013 08:32:00 -0000
X-Bugzilla-Reason: CC
X-Bugzilla-Type: changed
X-Bugzilla-Watch-Reason: None
X-Bugzilla-Product: gcc
X-Bugzilla-Component: tree-optimization
X-Bugzilla-Version: 4.9.0
X-Bugzilla-Keywords:
X-Bugzilla-Severity: normal
X-Bugzilla-Who: mpolacek at gcc dot gnu.org
X-Bugzilla-Status: NEW
X-Bugzilla-Priority: P3
X-Bugzilla-Assigned-To: unassigned at gcc dot gnu.org
X-Bugzilla-Target-Milestone: ---
X-Bugzilla-Flags:
X-Bugzilla-Changed-Fields: bug_status cf_reconfirmed_on cc short_desc everconfirmed
Message-ID: <bug-58653-4-DTxuGuGcS4@http.gcc.gnu.org/bugzilla/>
In-Reply-To: <bug-58653-4@http.gcc.gnu.org/bugzilla/>
References: <bug-58653-4@http.gcc.gnu.org/bugzilla/>
Content-Type: text/plain; charset="UTF-8"
Content-Transfer-Encoding: 7bit
X-Bugzilla-URL: http://gcc.gnu.org/bugzilla/
Auto-Submitted: auto-generated
MIME-Version: 1.0
X-SW-Source: 2013-10/txt/msg00378.txt.bz2
Content-length: 923
http://gcc.gnu.org/bugzilla/show_bug.cgi?idX653
Marek Polacek <mpolacek at gcc dot gnu.org> changed:
What |Removed |Added
----------------------------------------------------------------------------
Status|UNCONFIRMED |NEW
Last reconfirmed| |2013-10-07
CC| |mpolacek at gcc dot gnu.org
Summary|wrong code (segfaults) at |[4.7/4.8/4.9 Regression]
|-O3 on x86_64-linux-gnu in |wrong code (segfaults) at
|64-bit mode (affecting gcc |-O3 on x86_64-linux-gnu in
|4.6 to trunk) |64-bit mode (affecting gcc
| |4.6 to trunk)
Ever confirmed|0 |1
--- Comment #1 from Marek Polacek <mpolacek at gcc dot gnu.org> ---
Confirmed.
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (13 preceding siblings ...)
2013-10-07 8:12 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 10:14 ` vincenzo.innocente at cern dot ch
2013-10-07 10:28 ` jakub at gcc dot gnu.org
` (11 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 10:14 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #16 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
./affinity-1.exe
Initial thread
#1 thread 1
#1 thread 0
#1 thread 3
#1 thread 2
#1,#1 thread 3,1
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#2 thread 3,4
#1,#2 thread 3,0
#1,#2 thread 3,1
#1,#2 thread 3,3
#1,#2 thread 3,2
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,1
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,3
#1,#3 thread 3,2
#1,#3 thread 3,3
#1,#3 thread 3,1
#1,#3 thread 3,0
#1,#4 thread 3,2
#1,#4 thread 3,5
#1,#4 thread 3,4
#1,#4 thread 3,1
#1,#4 thread 3,3
#1,#4 thread 3,0
#2 thread 3
#2 thread 0
#2 thread 1
#2 thread 2
#2 thread 4
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,1
#2,#2 thread 3,2
#2,#2 thread 3,3
#2,#2 thread 3,4
#2,#3 thread 3,0
#2,#3 thread 3,1
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#4 thread 3,2
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,5
#2,#4 thread 3,1
#2,#4 thread 3,0
#3 thread 1
#3 thread 0
#3 thread 2
#3,#1 thread 2,1
#3,#1 thread 2,3
#3,#1 thread 2,0
#3,#1 thread 2,2
#3,#2 thread 2,1
#3,#2 thread 2,3
#3,#2 thread 2,0
#3,#2 thread 2,2
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,1
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,1
#3,#2,#2 thread 2,3,2
#3,#3 thread 2,0
#3,#3 thread 2,1
#3,#3 thread 2,2
#3,#3 thread 2,3
#3,#4 thread 2,2
#3,#4 thread 2,0
#3,#4 thread 2,5
#3,#4 thread 2,3
#3,#4 thread 2,4
#3,#4 thread 2,1
#4 thread 3
#4 thread 2
#4 thread 4
#4 thread 1
#4 thread 0
#4,#1 thread 2,0
#4,#1 thread 2,2
#4,#1 thread 2,3
#4,#1 thread 2,1
#4,#2 thread 2,2
#4,#2 thread 2,0
#4,#2 thread 2,1
#4,#2 thread 2,3
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,1
#4,#2,#2 thread 2,2,1
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,0
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,3
#4,#2,#3 thread 2,3,1
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,4
#4,#3 thread 2,2
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,1
#4,#4 thread 2,1
#4,#4 thread 2,2
#4,#4 thread 2,0
#4,#4 thread 2,5
#4,#4 thread 2,4
#4,#4 thread 2,3
[innocent@olsnba04 parallel]$ setenv OMP_PROC_BIND false
[innocent@olsnba04 parallel]$ ./affinity-1.exe
OMP_PROC_BIND='false'
Initial thread
#1 thread 1
#1 thread 3
#1 thread 2
#1 thread 0
#1,#1 thread 3,0
#1,#1 thread 3,1
#1,#1 thread 3,2
#1,#2 thread 3,1
#1,#2 thread 3,3
#1,#2 thread 3,0
#1,#2 thread 3,4
#1,#2 thread 3,2
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,1
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,2
#1,#3 thread 3,1
#1,#3 thread 3,3
#1,#3 thread 3,0
#1,#3 thread 3,2
#1,#4 thread 3,0
#1,#4 thread 3,5
#1,#4 thread 3,4
#1,#4 thread 3,3
#1,#4 thread 3,2
#1,#4 thread 3,1
#2 thread 0
#2 thread 4
#2 thread 3
#2 thread 2
#2 thread 1
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,2
#2,#2 thread 3,3
#2,#2 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,4
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#3 thread 3,0
#2,#4 thread 3,4
#2,#4 thread 3,5
#2,#4 thread 3,3
#2,#4 thread 3,1
#2,#4 thread 3,0
#2,#4 thread 3,2
#3 thread 1
#3 thread 2
#3 thread 0
#3,#1 thread 2,1
#3,#1 thread 2,2
#3,#1 thread 2,3
#3,#1 thread 2,0
#3,#2 thread 2,0
#3,#2 thread 2,1
#3,#2 thread 2,2
#3,#2 thread 2,3
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,1
#3,#2,#1 thread 2,0,0
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,1
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#3 thread 2,3
#3,#3 thread 2,0
#3,#4 thread 2,3
#3,#4 thread 2,1
#3,#4 thread 2,4
#3,#4 thread 2,2
#3,#4 thread 2,0
#3,#4 thread 2,5
#4 thread 3
#4 thread 2
#4 thread 1
#4 thread 4
#4 thread 0
#4,#1 thread 2,0
#4,#1 thread 2,1
#4,#1 thread 2,2
#4,#1 thread 2,3
#4,#2 thread 2,0
#4,#2 thread 2,2
#4,#2 thread 2,1
#4,#2 thread 2,3
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,1
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,4
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,1
#4,#2,#3 thread 2,3,1
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,3
#4,#3 thread 2,1
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#4 thread 2,0
#4,#4 thread 2,3
#4,#4 thread 2,4
#4,#4 thread 2,5
#4,#4 thread 2,2
#4,#4 thread 2,1
[innocent@olsnba04 parallel]$
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (14 preceding siblings ...)
2013-10-07 10:14 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 10:28 ` jakub at gcc dot gnu.org
2013-10-07 11:03 ` vincenzo.innocente at cern dot ch
` (10 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-07 10:28 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #17 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
(In reply to vincenzo Innocente from comment #16)
> [innocent@olsnba04 parallel]$ setenv OMP_PROC_BIND false
> [innocent@olsnba04 parallel]$ ./affinity-1.exe
> OMP_PROC_BIND='false'
> Initial thread
> #1 thread 1
> #1 thread 3
> #1 thread 2
> #1 thread 0
...
Thanks, though not what I was hoping to see. What glibc do you have on the
build box where you compiled the testcase? If it is too old (doesn't have
CPU_ALLOC_SIZE macro defined), or -DINTERPOSE_GETAFFINITY -DDO_FORK isn't
defined, or config.h doesn't defined HAVE_PTHREAD_AFFINITY_NP, then that's
expected. Or is the output running under taskset -c 0-3 ? The test verifies
things only if the initial affinity bitmask contains at least logical CPUs from
0 to 7 inclusive.
What I'm getting and expect is something like:
OMP_PROC_BIND='true' OMP_PLACES='{0,1},{3,2,4},{6,5,!6},{6},{7:2:-1,!6}'
Initial thread bound to {0:2}, verified
#1 thread 2 bound to {5}
#1 thread 0 bound to {0:2}
#1 thread 3 bound to {6}
#1 thread 1 bound to {2:3}
...
#1,#4 thread 3,5 bound to {6}
#2 thread 0 bound to {0:2}, verified
#2 thread 2 bound to {5}, verified
#2 thread 1 bound to {2:3}, verified
...
#4,#4 thread 2,0 bound to {5}, verified
#4,#4 thread 2,5 bound to {5}, verified
OMP_PROC_BIND='true' OMP_PLACES='{1}:7:1'
Initial thread bound to {1}, verified
...
(", verified" shouldn't be on lines starting with #1 if the header says
OMP_PROC_BIND='true').
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (15 preceding siblings ...)
2013-10-07 10:28 ` jakub at gcc dot gnu.org
@ 2013-10-07 11:03 ` vincenzo.innocente at cern dot ch
2013-10-07 11:06 ` vincenzo.innocente at cern dot ch
` (9 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 11:03 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #18 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
On 7 Oct, 2013, at 12:27 PM, jakub at gcc dot gnu.org
<gcc-bugzilla@gcc.gnu.org> wrote:
> http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
>
> --- Comment #17 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
> (In reply to vincenzo Innocente from comment #16)
>> [innocent@olsnba04 parallel]$ setenv OMP_PROC_BIND false
>> [innocent@olsnba04 parallel]$ ./affinity-1.exe
>> OMP_PROC_BIND='false'
>> Initial thread
>> #1 thread 1
>> #1 thread 3
>> #1 thread 2
>> #1 thread 0
> ...
>
> Thanks, though not what I was hoping to see. What glibc do you have on the
> build box where you compiled the testcase?
on the build machine
[innocent@vinavx0 testsuite]$ /home/data/newsoft/gcc-build/gcc/xgcc
-B/home/data/newsoft/gcc-build/gcc/
/home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c
-B/home/data/newsoft/gcc-build/x86_64-unknown-linux-gnu/./libgomp/
-B/home/data/newsoft/gcc-build/x86_64-unknown-linux-gnu/./libgomp/.libs
-I/home/data/newsoft/gcc-build/x86_64-unknown-linux-gnu/./libgomp
-I/home/data/newsoft/gcc-gomp4/libgomp/testsuite/.. -fmessage-length=0
-fno-diagnostics-show-caret -fopenmp -O2 -DINTERPOSE_GETAFFINITY -DDO_FORK
-ldl -L/home/data/newsoft/gcc-build/x86_64-unknown-linux-gnu/./libgomp/.libs
-lm -o ./affinity-1.exe
[innocent@vinavx0 testsuite]$ ls
Makefile affinity-1.exe libgomp.log libgomp.sum site.exp
[innocent@vinavx0 testsuite]$ ./affinity-1.exe
Initial thread bound to {0:8}
#1 thread 1 bound to {0:8}
#1 thread 3 bound to {0:8}
#1 thread 0 bound to {0:8}
#1 thread 2 bound to {0:8}
#1,#1 thread 3,1 bound to {0:8}
#1,#1 thread 3,0 bound to {0:8}
#1,#1 thread 3,2 bound to {0:8}
#1,#2 thread 3,3 bound to {0:8}
#1,#2 thread 3,1 bound to {0:8}
#1,#2 thread 3,0 bound to {0:8}
#1,#2 thread 3,2 bound to {0:8}
#1,#2 thread 3,4 bound to {0:8}
#1,#2,#1 thread 3,3,0 bound to {0:8}
#1,#2,#1 thread 3,3,4 bound to {0:8}
#1,#2,#1 thread 3,3,2 bound to {0:8}
#1,#2,#1 thread 3,3,3 bound to {0:8}
#1,#2,#1 thread 3,3,1 bound to {0:8}
#1,#3 thread 3,0 bound to {0:8}
#1,#3 thread 3,1 bound to {0:8}
#1,#3 thread 3,3 bound to {0:8}
#1,#3 thread 3,2 bound to {0:8}
#1,#4 thread 3,1 bound to {0:8}
#1,#4 thread 3,5 bound to {0:8}
#1,#4 thread 3,2 bound to {0:8}
#1,#4 thread 3,3 bound to {0:8}
#1,#4 thread 3,0 bound to {0:8}
#1,#4 thread 3,4 bound to {0:8}
#2 thread 0 bound to {0:8}
#2 thread 2 bound to {0:8}
#2 thread 4 bound to {0:8}
#2 thread 1 bound to {0:8}
#2 thread 3 bound to {0:8}
#2,#1 thread 3,0 bound to {0:8}
#2,#1 thread 3,2 bound to {0:8}
#2,#1 thread 3,1 bound to {0:8}
#2,#2 thread 3,2 bound to {0:8}
#2,#2 thread 3,1 bound to {0:8}
#2,#2 thread 3,4 bound to {0:8}
#2,#2 thread 3,3 bound to {0:8}
#2,#2 thread 3,0 bound to {0:8}
#2,#3 thread 3,2 bound to {0:8}
#2,#3 thread 3,0 bound to {0:8}
#2,#3 thread 3,1 bound to {0:8}
#2,#3 thread 3,3 bound to {0:8}
#2,#4 thread 3,2 bound to {0:8}
#2,#4 thread 3,0 bound to {0:8}
#2,#4 thread 3,1 bound to {0:8}
#2,#4 thread 3,4 bound to {0:8}
#2,#4 thread 3,5 bound to {0:8}
#2,#4 thread 3,3 bound to {0:8}
#3 thread 1 bound to {0:8}
#3 thread 2 bound to {0:8}
#3 thread 0 bound to {0:8}
#3,#1 thread 2,2 bound to {0:8}
#3,#1 thread 2,0 bound to {0:8}
#3,#1 thread 2,3 bound to {0:8}
#3,#1 thread 2,1 bound to {0:8}
#3,#2 thread 2,1 bound to {0:8}
#3,#2 thread 2,3 bound to {0:8}
#3,#2 thread 2,2 bound to {0:8}
#3,#2 thread 2,0 bound to {0:8}
#3,#2,#1 thread 2,0,1 bound to {0:8}
#3,#2,#1 thread 2,0,0 bound to {0:8}
#3,#2,#1 thread 2,0,2 bound to {0:8}
#3,#2,#1 thread 2,0,3 bound to {0:8}
#3,#2,#1 thread 2,0,4 bound to {0:8}
#3,#2,#2 thread 2,3,1 bound to {0:8}
#3,#2,#2 thread 2,3,0 bound to {0:8}
#3,#2,#2 thread 2,3,2 bound to {0:8}
#3,#2,#2 thread 2,3,3 bound to {0:8}
#3,#2,#2 thread 2,3,4 bound to {0:8}
#3,#3 thread 2,1 bound to {0:8}
#3,#3 thread 2,0 bound to {0:8}
#3,#3 thread 2,3 bound to {0:8}
#3,#3 thread 2,2 bound to {0:8}
#3,#4 thread 2,0 bound to {0:8}
#3,#4 thread 2,3 bound to {0:8}
#3,#4 thread 2,4 bound to {0:8}
#3,#4 thread 2,2 bound to {0:8}
#3,#4 thread 2,5 bound to {0:8}
#3,#4 thread 2,1 bound to {0:8}
#4 thread 3 bound to {0:8}
#4 thread 1 bound to {0:8}
#4 thread 4 bound to {0:8}
#4 thread 2 bound to {0:8}
#4 thread 0 bound to {0:8}
#4,#1 thread 2,2 bound to {0:8}
#4,#1 thread 2,0 bound to {0:8}
#4,#1 thread 2,3 bound to {0:8}
#4,#1 thread 2,1 bound to {0:8}
#4,#2 thread 2,2 bound to {0:8}
#4,#2 thread 2,3 bound to {0:8}
#4,#2 thread 2,0 bound to {0:8}
#4,#2 thread 2,1 bound to {0:8}
#4,#2,#1 thread 2,0,0 bound to {0:8}
#4,#2,#1 thread 2,0,3 bound to {0:8}
#4,#2,#1 thread 2,0,2 bound to {0:8}
#4,#2,#1 thread 2,0,1 bound to {0:8}
#4,#2,#1 thread 2,0,4 bound to {0:8}
#4,#2,#2 thread 2,2,1 bound to {0:8}
#4,#2,#2 thread 2,2,2 bound to {0:8}
#4,#2,#2 thread 2,2,0 bound to {0:8}
#4,#2,#2 thread 2,2,3 bound to {0:8}
#4,#2,#2 thread 2,2,4 bound to {0:8}
#4,#2,#3 thread 2,3,1 bound to {0:8}
#4,#2,#3 thread 2,3,4 bound to {0:8}
#4,#2,#3 thread 2,3,0 bound to {0:8}
#4,#2,#3 thread 2,3,2 bound to {0:8}
#4,#2,#3 thread 2,3,3 bound to {0:8}
#4,#3 thread 2,0 bound to {0:8}
#4,#3 thread 2,2 bound to {0:8}
#4,#3 thread 2,3 bound to {0:8}
#4,#3 thread 2,1 bound to {0:8}
#4,#4 thread 2,1 bound to {0:8}
#4,#4 thread 2,2 bound to {0:8}
#4,#4 thread 2,5 bound to {0:8}
#4,#4 thread 2,3 bound to {0:8}
#4,#4 thread 2,0 bound to {0:8}
#4,#4 thread 2,4 bound to {0:8}
[innocent@vinavx0 testsuite]$ cp ~/public/ctest/pa
parallel/ partialSum.cc
[innocent@vinavx0 testsuite]$ cp ~/public/ctest/parallel/./affinity-1.exe
cp: missing destination file operand after
`/afs/cern.ch/user/i/innocent/public/ctest/parallel/./affinity-1.exe'
Try `cp --help' for more information.
[innocent@vinavx0 testsuite]$ cp ~/public/ctest/parallel/affinity-1.exe .
cp: cannot stat
`/afs/cern.ch/user/i/innocent/public/ctest/parallel/affinity-1.exe': No such
file or directory
[innocent@vinavx0 testsuite]$ cp aff ~/public/ctest/parallel/.
Makefile affinity-1.exe* libgomp.log* libgomp.sum site.exp
[innocent@vinavx0 testsuite]$ cp affinity-1.exe ~/public/ctest/parallel/.
[innocent@vinavx0 testsuite]$ ldd ./affinity-1.exe
linux-vdso.so.1 => (0x00007fff44101000)
libdl.so.2 => /afs/cern.ch/user/i/innocent/w2/lib/libdl.so.2
(0x00007f03f5ee6000)
libm.so.6 => /afs/cern.ch/user/i/innocent/w2/lib/libm.so.6
(0x00007f03f5c68000)
libgomp.so.1 => /afs/cern.ch/user/i/innocent/w2/lib64/libgomp.so.1
(0x00007f03f5a51000)
libpthread.so.0 => /afs/cern.ch/user/i/innocent/w2/lib/libpthread.so.0
(0x00007f03f5834000)
libc.so.6 => /afs/cern.ch/user/i/innocent/w2/lib/libc.so.6
(0x00007f03f54ab000)
/lib64/ld-linux-x86-64.so.2 (0x0000003672000000)
librt.so.1 => /afs/cern.ch/user/i/innocent/w2/lib/librt.so.1
(0x00007f03f5290000)
on the XEON
ldd ./affinity-1.exe
linux-vdso.so.1 => (0x00007fff28ffe000)
libdl.so.2 => /afs/cern.ch/user/i/innocent/w2/lib/libdl.so.2
(0x00007f49aef18000)
libm.so.6 => /afs/cern.ch/user/i/innocent/w2/lib/libm.so.6
(0x00007f49aec9a000)
libgomp.so.1 => /afs/cern.ch/user/i/innocent/w2/lib64/libgomp.so.1
(0x00007f49aea83000)
libpthread.so.0 => /afs/cern.ch/user/i/innocent/w2/lib/libpthread.so.0
(0x00007f49ae866000)
libc.so.6 => /afs/cern.ch/user/i/innocent/w2/lib/libc.so.6
(0x00007f49ae4dd000)
/lib64/ld-linux-x86-64.so.2 (0x000000320e800000)
librt.so.1 => /afs/cern.ch/user/i/innocent/w2/lib/librt.so.1
(0x00007f49ae2c2000)
[innocent@olsnba04 parallel]$ /afs/cern.ch/user/i/innocent/w2/lib/libc.so.6
GNU C Library stable release version 2.13, by Roland McGrath et al.
Copyright (C) 2011 Free Software Foundation, Inc.
This is free software; see the source for copying conditions.
There is NO warranty; not even for MERCHANTABILITY or FITNESS FOR A
PARTICULAR PURPOSE.
Compiled by GNU CC version 4.6.1 20110520 (prerelease).
Compiled on a Linux 2.6.32 system on 2011-05-30.
Available extensions:
crypt add-on version 2.1 by Michael Glad and others
GNU Libidn by Simon Josefsson
Native POSIX Threads Library by Ulrich Drepper et al
BIND-8.2.3-T5B
libc ABIs: UNIQUE IFUNC
For bug reporting instructions, please see:
<http://www.gnu.org/software/libc/bugs.html>.
> If it is too old (doesn't have
> CPU_ALLOC_SIZE macro defined), or -DINTERPOSE_GETAFFINITY -DDO_FORK isn't
> defined, or config.h doesn't defined HAVE_PTHREAD_AFFINITY_NP, then that's
> expected. Or is the output running under taskset -c 0-3 ?
no
> The test verifies
> things only if the initial affinity bitmask contains at least logical CPUs from
> 0 to 7 inclusive.
> What I'm getting and expect is something like:
> OMP_PROC_BIND='true' OMP_PLACES='{0,1},{3,2,4},{6,5,!6},{6},{7:2:-1,!6}'
csh does not like "!"
echo $OMP_PLACES
0,3,6,6,7:2:-1 0,3,6,6,!6 0,3,5,6,7:2:-1 0,3,5,6,!6 0,3,!6,6,7:2:-1 0,3,!6,6,!6
0,2,6,6,7:2:-1 0,2,6,6,!6 0,2,5,6,7:2:-1 0,2,5,6,!6 0,2,!6,6,7:2:-1 0,2,!6,6,!6
0,4,6,6,7:2:-1 0,4,6,6,!6 0,4,5,6,7:2:-1 0,4,5,6,!6 0,4,!6,6,7:2:-1 0,4,!6,6,!6
1,3,6,6,7:2:-1 1,3,6,6,!6 1,3,5,6,7:2:-1 1,3,5,6,!6 1,3,!6,6,7:2:-1 1,3,!6,6,!6
1,2,6,6,7:2:-1 1,2,6,6,!6 1,2,5,6,7:2:-1 1,2,5,6,!6 1,2,!6,6,7:2:-1 1,2,!6,6,!6
1,4,6,6,7:2:-1 1,4,6,6,!6 1,4,5,6,7:2:-1 1,4,5,6,!6 1,4,!6,6,7:2:-1 1,4,!6,6,!6
in zsh
innocent@olsnba04]~/me/public/ctest/parallel% export OMP_PROC_BIND='true';
export OMP_PLACES='{0,1},{3,2,4},{6,5,!6},{6},{7:2:-1,!6}'
[innocent@olsnba04]~/me/public/ctest/parallel% ./affinity-1.exe
OMP_PROC_BIND='true' OMP_PLACES='{0,1},{3,2,4},{6,5,!6},{6},{7:2:-1,!6}'
Initial thread
#1 thread 0
#1 thread 2
#1 thread 3
#1 thread 1
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,3
#1,#2 thread 3,0
#1,#2 thread 3,4
#1,#2 thread 3,1
#1,#2 thread 3,2
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,4
#1,#4 thread 3,2
#1,#4 thread 3,0
#1,#4 thread 3,1
#1,#4 thread 3,3
#1,#4 thread 3,5
#2 thread 3
#2 thread 2
#2 thread 0
#2 thread 4
#2 thread 1
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,4
#2,#2 thread 3,3
#2,#2 thread 3,2
#2,#2 thread 3,1
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,0
#2,#4 thread 3,5
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,2
#2,#4 thread 3,1
#3 thread 1
#3 thread 0
#3 thread 2
#3,#1 thread 2,0
#3,#1 thread 2,1
#3,#1 thread 2,2
#3,#1 thread 2,3
#3,#2 thread 2,1
#3,#2 thread 2,2
#3,#2 thread 2,3
#3,#2 thread 2,0
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,1
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,1
#3,#3 thread 2,1
#3,#3 thread 2,2
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#4 thread 2,1
#3,#4 thread 2,2
#3,#4 thread 2,3
#3,#4 thread 2,5
#3,#4 thread 2,4
#3,#4 thread 2,0
#4 thread 1
#4 thread 2
#4 thread 4
#4 thread 3
#4 thread 0
#4,#1 thread 2,3
#4,#1 thread 2,1
#4,#1 thread 2,2
#4,#1 thread 2,0
#4,#2 thread 2,1
#4,#2 thread 2,3
#4,#2 thread 2,2
#4,#2 thread 2,0
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,1
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,1
#4,#2,#3 thread 2,3,1
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,3
#4,#2,#3 thread 2,3,0
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,1
#4,#4 thread 2,2
#4,#4 thread 2,3
#4,#4 thread 2,0
#4,#4 thread 2,4
#4,#4 thread 2,5
[innocent@olsnba04]~/me/public/ctest/parallel%
> Initial thread bound to {0:2}, verified
> #1 thread 2 bound to {5}
> #1 thread 0 bound to {0:2}
> #1 thread 3 bound to {6}
> #1 thread 1 bound to {2:3}
> ...
> #1,#4 thread 3,5 bound to {6}
> #2 thread 0 bound to {0:2}, verified
> #2 thread 2 bound to {5}, verified
> #2 thread 1 bound to {2:3}, verified
> ...
> #4,#4 thread 2,0 bound to {5}, verified
> #4,#4 thread 2,5 bound to {5}, verified
> OMP_PROC_BIND='true' OMP_PLACES='{1}:7:1'
> Initial thread bound to {1}, verified
> ...
> (", verified" shouldn't be on lines starting with #1 if the header says
> OMP_PROC_BIND='true').
>
> --
> You are receiving this mail because:
> You reported the bug.
--
Il est bon de suivre sa pente, pourvu que ce soit en montant.
A.G.
http://www.flickr.com/photos/vin60/1320965757/
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (16 preceding siblings ...)
2013-10-07 11:03 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 11:06 ` vincenzo.innocente at cern dot ch
2013-10-07 11:32 ` jakub at gcc dot gnu.org
` (8 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 11:06 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #19 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
On 7 Oct, 2013, at 12:27 PM, jakub at gcc dot gnu.org
<gcc-bugzilla@gcc.gnu.org> wrote:
> or config.h doesn't defined HAVE_PTHREAD_AFFINITY_NP, then that's
> expected.
innocent@vinavx0 testsuite]$ cat ../config.h
/* config.h. Generated from config.h.in by configure. */
/* config.h.in. Generated from configure.ac by autoheader. */
/* Define to 1 if the target assembler supports .symver directive. */
#define HAVE_AS_SYMVER_DIRECTIVE 1
/* Define to 1 if the target supports __attribute__((alias(...))). */
#define HAVE_ATTRIBUTE_ALIAS 1
/* Define to 1 if the target supports __attribute__((dllexport)). */
/* #undef HAVE_ATTRIBUTE_DLLEXPORT */
/* Define to 1 if the target supports __attribute__((visibility(...))). */
#define HAVE_ATTRIBUTE_VISIBILITY 1
/* Define if the POSIX Semaphores do not work on your system. */
/* #undef HAVE_BROKEN_POSIX_SEMAPHORES */
/* Define to 1 if the target assembler supports thread-local storage. */
/* #undef HAVE_CC_TLS */
/* Define to 1 if you have the `clock_gettime' function. */
#define HAVE_CLOCK_GETTIME 1
/* Define to 1 if you have the <dlfcn.h> header file. */
#define HAVE_DLFCN_H 1
/* Define to 1 if you have the `getloadavg' function. */
#define HAVE_GETLOADAVG 1
/* Define to 1 if you have the <inttypes.h> header file. */
#define HAVE_INTTYPES_H 1
/* Define to 1 if you have the `dl' library (-ldl). */
#define HAVE_LIBDL 1
/* Define to 1 if you have the <memory.h> header file. */
#define HAVE_MEMORY_H 1
/* Define if pthread_{,attr_}{g,s}etaffinity_np is supported. */
#define HAVE_PTHREAD_AFFINITY_NP 1
/* Define to 1 if you have the <semaphore.h> header file. */
#define HAVE_SEMAPHORE_H 1
/* Define to 1 if you have the <stdint.h> header file. */
#define HAVE_STDINT_H 1
/* Define to 1 if you have the <stdlib.h> header file. */
#define HAVE_STDLIB_H 1
/* Define to 1 if you have the <strings.h> header file. */
#define HAVE_STRINGS_H 1
/* Define to 1 if you have the <string.h> header file. */
#define HAVE_STRING_H 1
/* Define to 1 if you have the `strtoull' function. */
#define HAVE_STRTOULL 1
/* Define to 1 if the target runtime linker supports binding the same symbol
to different versions. */
#define HAVE_SYMVER_SYMBOL_RENAMING_RUNTIME_SUPPORT 1
/* Define to 1 if the target supports __sync_*_compare_and_swap */
#define HAVE_SYNC_BUILTINS 1
/* Define to 1 if you have the <sys/loadavg.h> header file. */
/* #undef HAVE_SYS_LOADAVG_H */
/* Define to 1 if you have the <sys/stat.h> header file. */
#define HAVE_SYS_STAT_H 1
/* Define to 1 if you have the <sys/time.h> header file. */
#define HAVE_SYS_TIME_H 1
/* Define to 1 if you have the <sys/types.h> header file. */
#define HAVE_SYS_TYPES_H 1
/* Define to 1 if the target supports thread-local storage. */
#define HAVE_TLS 1
/* Define to 1 if you have the <unistd.h> header file. */
#define HAVE_UNISTD_H 1
/* Define to 1 if GNU symbol versioning is used for libgomp. */
#define LIBGOMP_GNU_SYMBOL_VERSIONING 1
/* Define to the sub-directory in which libtool stores uninstalled libraries.
*/
#define LT_OBJDIR ".libs/"
/* Name of package */
#define PACKAGE "libgomp"
/* Define to the address where bug reports for this package should be sent. */
#define PACKAGE_BUGREPORT ""
/* Define to the full name of this package. */
#define PACKAGE_NAME "GNU OpenMP Runtime Library"
/* Define to the full name and version of this package. */
#define PACKAGE_STRING "GNU OpenMP Runtime Library 1.0"
/* Define to the one symbol short name of this package. */
#define PACKAGE_TARNAME "libgomp"
/* Define to the home page for this package. */
#define PACKAGE_URL "http://www.gnu.org/software/libgomp/"
/* Define to the version of this package. */
#define PACKAGE_VERSION "1.0"
/* Define if all infrastructure, needed for plugins, is supported. */
#define PLUGIN_SUPPORT 1
/* The size of `char', as computed by sizeof. */
/* #undef SIZEOF_CHAR */
/* The size of `int', as computed by sizeof. */
/* #undef SIZEOF_INT */
/* The size of `long', as computed by sizeof. */
/* #undef SIZEOF_LONG */
/* The size of `short', as computed by sizeof. */
/* #undef SIZEOF_SHORT */
/* The size of `void *', as computed by sizeof. */
/* #undef SIZEOF_VOID_P */
/* Define to 1 if you have the ANSI C header files. */
#define STDC_HEADERS 1
/* Define if you can safely include both <string.h> and <strings.h>. */
#define STRING_WITH_STRINGS 1
/* Define to 1 if you can safely include both <sys/time.h> and <time.h>. */
#define TIME_WITH_SYS_TIME 1
/* Version number of package */
#define VERSION "1.0"
--
Il est bon de suivre sa pente, pourvu que ce soit en montant.
A.G.
http://www.flickr.com/photos/vin60/1320965757/
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (17 preceding siblings ...)
2013-10-07 11:06 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 11:32 ` jakub at gcc dot gnu.org
2013-10-07 11:39 ` jakub at gcc dot gnu.org
` (7 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-07 11:32 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #20 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
I'll commit the patch anyway, it is a step forward.
Anyway, the way the testcase is written is that if you run it with
OMP_PROC_BIND=false in the environment and OMP_PLACES unset, then it should
fork and exec /proc/self/exe with various settings of those two environment
variables.
Can you perhaps see in the debugger what value has contig_cpucount variable at
the start of main, and why it decided not to fork (or, has it failed to exec
/proc/self/exe)?
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (18 preceding siblings ...)
2013-10-07 11:32 ` jakub at gcc dot gnu.org
@ 2013-10-07 11:39 ` jakub at gcc dot gnu.org
2013-10-07 12:07 ` vincenzo.innocente at cern dot ch
` (6 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-07 11:39 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #21 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
Author: jakub
Date: Mon Oct 7 11:39:39 2013
New Revision: 203243
URL: http://gcc.gnu.org/viewcvs?rev=203243&root=gcc&view=rev
Log:
PR libgomp/58642
* config/linux/proc.c: Include errno.h.
(gomp_get_cpuset_size): New variable.
(gomp_cpuset_popcount): Add cpusetsize argument, use it instead of
gomp_cpuset_size.
(gomp_init_num_threads): If CPU_ALLOC_SIZE is defined and
pthread_getaffinity_np returned EINVAL, increase gomp_cpuset_size
and retry. After successful pthread_getaffinity_np copy
gomp_cpuset_size to gomp_get_cpuset_size and try to find out
minimum gomp_cpuset_size that covers all the CPUs set in gomp_cpusetp.
(get_num_procs): Pass gomp_get_cpuset_size rather than gomp_cpuset_size
to pthread_getaffinity_np, adjust gomp_cpuset_popcount caller.
* config/linux/proc.h (gomp_cpuset_popcount): Add cpusetsize argument.
* config/linux/affinity.c (gomp_affinity_finalize_place_list,
gomp_affinity_init_level): Adjust gomp_cpuset_popcount callers.
* testsuite/libgomp.c/affinity-1.c (pthread_getaffinity_np): Set
contig_cpucount from the first successful pthread_getaffinity_np
call, rather than just first call.
Modified:
branches/gomp-4_0-branch/libgomp/ChangeLog.gomp
branches/gomp-4_0-branch/libgomp/config/linux/affinity.c
branches/gomp-4_0-branch/libgomp/config/linux/proc.c
branches/gomp-4_0-branch/libgomp/config/linux/proc.h
branches/gomp-4_0-branch/libgomp/testsuite/libgomp.c/affinity-1.c
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (19 preceding siblings ...)
2013-10-07 11:39 ` jakub at gcc dot gnu.org
@ 2013-10-07 12:07 ` vincenzo.innocente at cern dot ch
2013-10-07 12:43 ` vincenzo.innocente at cern dot ch
` (5 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 12:07 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #22 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
on the XEON
setenv OMP_PROC_BIND false
reakpoint 1, main () at
/home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:181
181 /home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:
No such file or directory.
in /home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c
Missing separate debuginfos, use: debuginfo-install
glibc-2.12-1.107.el6_4.4.x86_64
(gdb) print contig_cpucount
$1 = 32
it fork only if it is 8…
(ok on the build machine indeed)
180 #ifdef DO_FORK
181 if (env_places == NULL && contig_cpucount == 8 && test_false
182 && getenv ("GOMP_AFFINITY") == NULL)
so (see below full output )
taskset -c 0-7 gdb ./affinity-1.exe
GNU gdb (GDB) Red Hat Enterprise Linux (7.2-60.el6_4.1)
(gdb) b
/home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:179
Breakpoint 1 at 0x400d5f: file
/home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c, line
179.
(gdb) run
Starting program:
/afs/cern.ch/user/i/innocent/public/ctest/parallel/affinity-1.exe
warning: no loadable sections found in added symbol-file system-supplied DSO at
0x7ffff7ffd000
[Thread debugging using libthread_db enabled]
Breakpoint 1, main () at
/home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:181
181 /home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:
No such file or directory.
in /home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c
Missing separate debuginfos, use: debuginfo-install
glibc-2.12-1.107.el6_4.4.x86_64
(gdb) print contig_cpucount
$1 = 8
BUT
taskset -c 24-31 gdb ./affinity-1.exe
Breakpoint 1, main () at
/home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:181
181 /home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:
No such file or directory.
in /home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c
Missing separate debuginfos, use: debuginfo-install
glibc-2.12-1.107.el6_4.4.x86_64
(gdb) print contig_cpucount
$1 = 0
taskset -c 0-7 ./affinity-1.exe
libgomp: Number of places reduced from 5 to 1 because some places didn't
contain any usable logical CPUs
OMP_PROC_BIND='true' OMP_PLACES='{0,1},{3,2,4},{6,5,!6},{6},{7:2:-1,!6}'
Initial thread
#1 thread 0
#1 thread 3
#1 thread 2
#1 thread 1
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,0
#1,#2 thread 3,4
#1,#2 thread 3,3
#1,#2 thread 3,2
#1,#2 thread 3,1
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,0
#1,#4 thread 3,5
#1,#4 thread 3,4
#1,#4 thread 3,3
#1,#4 thread 3,2
#1,#4 thread 3,1
#2 thread 3
#2 thread 0
#2 thread 2
#2 thread 1
#2 thread 4
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,4
#2,#2 thread 3,3
#2,#2 thread 3,2
#2,#2 thread 3,1
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,0
#2,#4 thread 3,5
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,2
#2,#4 thread 3,1
#3 thread 1
#3 thread 2
#3 thread 0
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,0
#3,#2 thread 2,3
#3,#2 thread 2,2
#3,#2 thread 2,1
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,1
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,1
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#4 thread 2,0
#3,#4 thread 2,5
#3,#4 thread 2,4
#3,#4 thread 2,3
#3,#4 thread 2,2
#3,#4 thread 2,1
#4 thread 2
#4 thread 0
#4 thread 1
#4 thread 4
#4 thread 3
#4,#1 thread 2,0
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,1
#4,#2 thread 2,0
#4,#2 thread 2,3
#4,#2 thread 2,2
#4,#2 thread 2,1
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,1
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,1
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,3
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,1
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,0
#4,#4 thread 2,5
#4,#4 thread 2,4
#4,#4 thread 2,3
#4,#4 thread 2,2
#4,#4 thread 2,1
libgomp: None of the places contain usable logical CPUs
libgomp: Invalid value for environment variable OMP_PLACES
OMP_PROC_BIND='true' OMP_PLACES='{1}:7:1'
Initial thread
#1 thread 1
#1 thread 2
#1 thread 0
#1 thread 3
#1,#1 thread 3,2
#1,#1 thread 3,0
#1,#1 thread 3,1
#1,#2 thread 3,4
#1,#2 thread 3,2
#1,#2 thread 3,3
#1,#2 thread 3,1
#1,#2 thread 3,0
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,5
#1,#4 thread 3,4
#1,#4 thread 3,2
#1,#4 thread 3,3
#1,#4 thread 3,0
#1,#4 thread 3,1
#2 thread 4
#2 thread 1
#2 thread 2
#2 thread 0
#2 thread 3
#2,#1 thread 3,2
#2,#1 thread 3,0
#2,#1 thread 3,1
#2,#2 thread 3,1
#2,#2 thread 3,4
#2,#2 thread 3,0
#2,#2 thread 3,3
#2,#2 thread 3,2
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,5
#2,#4 thread 3,0
#2,#4 thread 3,3
#2,#4 thread 3,2
#2,#4 thread 3,4
#2,#4 thread 3,1
#3 thread 0
#3 thread 2
#3 thread 1
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,3
#3,#2 thread 2,2
#3,#2 thread 2,1
#3,#2 thread 2,0
#3,#2,#1 thread 2,0,1
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,2
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,1
#3,#2,#2 thread 2,3,3
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#4 thread 2,1
#3,#4 thread 2,0
#3,#4 thread 2,2
#3,#4 thread 2,5
#3,#4 thread 2,3
#3,#4 thread 2,4
#4 thread 1
#4 thread 2
#4 thread 3
#4 thread 4
#4 thread 0
#4,#1 thread 2,1
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,0
#4,#2 thread 2,2
#4,#2 thread 2,1
#4,#2 thread 2,3
#4,#2 thread 2,0
#4,#2,#1 thread 2,0,1
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,0
#4,#2,#2 thread 2,2,1
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,1
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,3
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,1
#4,#4 thread 2,2
#4,#4 thread 2,3
#4,#4 thread 2,5
#4,#4 thread 2,0
#4,#4 thread 2,4
libgomp: Number of places reduced from 3 to 1 because some places didn't
contain any usable logical CPUs
OMP_PROC_BIND='true' OMP_PLACES='{6,7}:4:-2,!{2,3}'
Initial thread
#1 thread 0
#1 thread 3
#1 thread 2
#1 thread 1
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,0
#1,#2 thread 3,4
#1,#2 thread 3,3
#1,#2 thread 3,2
#1,#2 thread 3,1
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,0
#1,#4 thread 3,5
#1,#4 thread 3,4
#1,#4 thread 3,3
#1,#4 thread 3,2
#1,#4 thread 3,1
#2 thread 3
#2 thread 0
#2 thread 2
#2 thread 1
#2 thread 4
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,4
#2,#2 thread 3,3
#2,#2 thread 3,2
#2,#2 thread 3,1
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,0
#2,#4 thread 3,5
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,2
#2,#4 thread 3,1
#3 thread 2
#3 thread 1
#3 thread 0
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,0
#3,#2 thread 2,3
#3,#2 thread 2,2
#3,#2 thread 2,1
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,1
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,1
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#4 thread 2,0
#3,#4 thread 2,5
#3,#4 thread 2,4
#3,#4 thread 2,3
#3,#4 thread 2,2
#3,#4 thread 2,1
#4 thread 2
#4 thread 0
#4 thread 1
#4 thread 4
#4 thread 3
#4,#1 thread 2,0
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,1
#4,#2 thread 2,0
#4,#2 thread 2,3
#4,#2 thread 2,2
#4,#2 thread 2,1
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,1
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,1
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,3
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,1
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,0
#4,#4 thread 2,5
#4,#4 thread 2,4
#4,#4 thread 2,3
#4,#4 thread 2,2
#4,#4 thread 2,1
libgomp: None of the places contain usable logical CPUs
libgomp: Invalid value for environment variable OMP_PLACES
OMP_PROC_BIND='true' OMP_PLACES='{7,6}:2:-3'
Initial thread
#1 thread 1
#1 thread 0
#1 thread 2
#1 thread 3
#1,#1 thread 3,2
#1,#1 thread 3,0
#1,#1 thread 3,1
#1,#2 thread 3,4
#1,#2 thread 3,0
#1,#2 thread 3,2
#1,#2 thread 3,1
#1,#2 thread 3,3
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,1
#1,#4 thread 3,2
#1,#4 thread 3,4
#1,#4 thread 3,3
#1,#4 thread 3,5
#1,#4 thread 3,0
#2 thread 4
#2 thread 1
#2 thread 2
#2 thread 0
#2 thread 3
#2,#1 thread 3,2
#2,#1 thread 3,0
#2,#1 thread 3,1
#2,#2 thread 3,1
#2,#2 thread 3,4
#2,#2 thread 3,2
#2,#2 thread 3,0
#2,#2 thread 3,3
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,3
#2,#4 thread 3,4
#2,#4 thread 3,0
#2,#4 thread 3,5
#2,#4 thread 3,1
#2,#4 thread 3,2
#3 thread 0
#3 thread 2
#3 thread 1
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,1
#3,#2 thread 2,3
#3,#2 thread 2,0
#3,#2 thread 2,2
#3,#2,#1 thread 2,0,1
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,2
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,1
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,4
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#4 thread 2,1
#3,#4 thread 2,0
#3,#4 thread 2,2
#3,#4 thread 2,4
#3,#4 thread 2,3
#3,#4 thread 2,5
#4 thread 1
#4 thread 2
#4 thread 4
#4 thread 3
#4 thread 0
#4,#1 thread 2,1
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,0
#4,#2 thread 2,3
#4,#2 thread 2,1
#4,#2 thread 2,2
#4,#2 thread 2,0
#4,#2,#1 thread 2,0,1
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,0
#4,#2,#2 thread 2,2,1
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,0
#4,#2,#3 thread 2,3,1
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,3
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,1
#4,#4 thread 2,2
#4,#4 thread 2,3
#4,#4 thread 2,5
#4,#4 thread 2,0
#4,#4 thread 2,4
libgomp: Number of places reduced from 8 to 1 because some places didn't
contain any usable logical CPUs
OMP_PROC_BIND='true' OMP_PLACES='{0}:8'
Initial thread
#1 thread 0
#1 thread 3
#1 thread 2
#1 thread 1
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,0
#1,#2 thread 3,4
#1,#2 thread 3,3
#1,#2 thread 3,2
#1,#2 thread 3,1
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,0
#1,#4 thread 3,5
#1,#4 thread 3,4
#1,#4 thread 3,3
#1,#4 thread 3,2
#1,#4 thread 3,1
#2 thread 3
#2 thread 0
#2 thread 2
#2 thread 1
#2 thread 4
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,4
#2,#2 thread 3,3
#2,#2 thread 3,2
#2,#2 thread 3,1
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,0
#2,#4 thread 3,5
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,2
#2,#4 thread 3,1
#3 thread 2
#3 thread 1
#3 thread 0
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,0
#3,#2 thread 2,3
#3,#2 thread 2,2
#3,#2 thread 2,1
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,1
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,1
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#4 thread 2,0
#3,#4 thread 2,5
#3,#4 thread 2,4
#3,#4 thread 2,3
#3,#4 thread 2,2
#3,#4 thread 2,1
#4 thread 2
#4 thread 0
#4 thread 1
#4 thread 4
#4 thread 3
#4,#1 thread 2,0
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,1
#4,#2 thread 2,0
#4,#2 thread 2,3
#4,#2 thread 2,2
#4,#2 thread 2,1
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,1
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,1
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,3
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,1
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,0
#4,#4 thread 2,5
#4,#4 thread 2,4
#4,#4 thread 2,3
#4,#4 thread 2,2
#4,#4 thread 2,1
libgomp: Number of places reduced from 5 to 1 because some places didn't
contain any usable logical CPUs
OMP_PROC_BIND='spread,master,close'
OMP_PLACES='{0,1},{3,2,4},{6,5,!6},{6},{7:2:-1,!6}'
Initial thread
#1 thread 0
#1 thread 3
#1 thread 2
#1 thread 1
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,0
#1,#2 thread 3,4
#1,#2 thread 3,3
#1,#2 thread 3,2
#1,#2 thread 3,1
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,0
#1,#4 thread 3,5
#1,#4 thread 3,4
#1,#4 thread 3,3
#1,#4 thread 3,2
#1,#4 thread 3,1
#2 thread 3
#2 thread 0
#2 thread 2
#2 thread 1
#2 thread 4
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,4
#2,#2 thread 3,3
#2,#2 thread 3,2
#2,#2 thread 3,1
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,0
#2,#4 thread 3,5
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,2
#2,#4 thread 3,1
#3 thread 1
#3 thread 2
#3 thread 0
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,0
#3,#2 thread 2,3
#3,#2 thread 2,2
#3,#2 thread 2,1
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,1
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,1
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#4 thread 2,0
#3,#4 thread 2,5
#3,#4 thread 2,4
#3,#4 thread 2,3
#3,#4 thread 2,2
#3,#4 thread 2,1
#4 thread 2
#4 thread 0
#4 thread 1
#4 thread 4
#4 thread 3
#4,#1 thread 2,0
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,1
#4,#2 thread 2,0
#4,#2 thread 2,3
#4,#2 thread 2,2
#4,#2 thread 2,1
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,1
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,1
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,3
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,1
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,0
#4,#4 thread 2,5
#4,#4 thread 2,4
#4,#4 thread 2,3
#4,#4 thread 2,2
#4,#4 thread 2,1
libgomp: None of the places contain usable logical CPUs
libgomp: Invalid value for environment variable OMP_PLACES
OMP_PROC_BIND='spread,master,close' OMP_PLACES='{1}:7:1'
Initial thread
#1 thread 2
#1 thread 3
#1 thread 1
#1 thread 0
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,4
#1,#2 thread 3,1
#1,#2 thread 3,0
#1,#2 thread 3,3
#1,#2 thread 3,2
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,1
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,3
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,5
#1,#4 thread 3,0
#1,#4 thread 3,2
#1,#4 thread 3,1
#1,#4 thread 3,4
#1,#4 thread 3,3
#2 thread 4
#2 thread 0
#2 thread 2
#2 thread 3
#2 thread 1
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,3
#2,#2 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,2
#2,#2 thread 3,4
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,5
#2,#4 thread 3,0
#2,#4 thread 3,2
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,1
#3 thread 0
#3 thread 2
#3 thread 1
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,1
#3,#2 thread 2,3
#3,#2 thread 2,2
#3,#2 thread 2,0
#3,#2,#1 thread 2,0,1
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,4
#3,#2,#2 thread 2,3,1
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,3
#3,#3 thread 2,0
#3,#3 thread 2,1
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#4 thread 2,1
#3,#4 thread 2,2
#3,#4 thread 2,4
#3,#4 thread 2,3
#3,#4 thread 2,0
#3,#4 thread 2,5
#4 thread 1
#4 thread 2
#4 thread 4
#4 thread 3
#4 thread 0
#4,#1 thread 2,0
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,1
#4,#2 thread 2,2
#4,#2 thread 2,3
#4,#2 thread 2,1
#4,#2 thread 2,0
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,1
#4,#2,#2 thread 2,2,1
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,3
#4,#2,#3 thread 2,3,1
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,3
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,5
#4,#4 thread 2,0
#4,#4 thread 2,1
#4,#4 thread 2,2
#4,#4 thread 2,4
#4,#4 thread 2,3
libgomp: Number of places reduced from 3 to 1 because some places didn't
contain any usable logical CPUs
OMP_PROC_BIND='spread,master,close' OMP_PLACES='{6,7}:4:-2,!{2,3}'
Initial thread
#1 thread 0
#1 thread 3
#1 thread 2
#1 thread 1
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,0
#1,#2 thread 3,4
#1,#2 thread 3,3
#1,#2 thread 3,2
#1,#2 thread 3,1
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,0
#1,#4 thread 3,5
#1,#4 thread 3,4
#1,#4 thread 3,3
#1,#4 thread 3,2
#1,#4 thread 3,1
#2 thread 3
#2 thread 0
#2 thread 2
#2 thread 1
#2 thread 4
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,4
#2,#2 thread 3,3
#2,#2 thread 3,2
#2,#2 thread 3,1
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,0
#2,#4 thread 3,5
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,2
#2,#4 thread 3,1
#3 thread 2
#3 thread 1
#3 thread 0
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,0
#3,#2 thread 2,3
#3,#2 thread 2,2
#3,#2 thread 2,1
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,1
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,1
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#4 thread 2,0
#3,#4 thread 2,5
#3,#4 thread 2,4
#3,#4 thread 2,3
#3,#4 thread 2,2
#3,#4 thread 2,1
#4 thread 2
#4 thread 0
#4 thread 1
#4 thread 4
#4 thread 3
#4,#1 thread 2,0
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,1
#4,#2 thread 2,0
#4,#2 thread 2,3
#4,#2 thread 2,2
#4,#2 thread 2,1
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,1
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,1
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,3
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,1
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,0
#4,#4 thread 2,5
#4,#4 thread 2,4
#4,#4 thread 2,3
#4,#4 thread 2,2
#4,#4 thread 2,1
libgomp: None of the places contain usable logical CPUs
libgomp: Invalid value for environment variable OMP_PLACES
OMP_PROC_BIND='spread,master,close' OMP_PLACES='{7,6}:2:-3'
Initial thread
#1 thread 3
#1 thread 1
#1 thread 2
#1 thread 0
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,4
#1,#2 thread 3,1
#1,#2 thread 3,0
#1,#2 thread 3,3
#1,#2 thread 3,2
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,5
#1,#4 thread 3,0
#1,#4 thread 3,2
#1,#4 thread 3,1
#1,#4 thread 3,4
#1,#4 thread 3,3
#2 thread 2
#2 thread 3
#2 thread 1
#2 thread 0
#2 thread 4
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,4
#2,#2 thread 3,0
#2,#2 thread 3,2
#2,#2 thread 3,1
#2,#2 thread 3,3
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,2
#2,#4 thread 3,5
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,0
#2,#4 thread 3,1
#3 thread 0
#3 thread 2
#3 thread 1
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,1
#3,#2 thread 2,3
#3,#2 thread 2,2
#3,#2 thread 2,0
#3,#2,#1 thread 2,0,1
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,4
#3,#2,#2 thread 2,3,1
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,3
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#4 thread 2,1
#3,#4 thread 2,5
#3,#4 thread 2,3
#3,#4 thread 2,0
#3,#4 thread 2,4
#3,#4 thread 2,2
#4 thread 1
#4 thread 2
#4 thread 3
#4 thread 4
#4 thread 0
#4,#1 thread 2,0
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,1
#4,#2 thread 2,3
#4,#2 thread 2,1
#4,#2 thread 2,2
#4,#2 thread 2,0
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,1
#4,#2,#1 thread 2,0,3
#4,#2,#2 thread 2,2,1
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,3
#4,#2,#3 thread 2,3,1
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,3
#4,#3 thread 2,1
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#4 thread 2,1
#4,#4 thread 2,3
#4,#4 thread 2,5
#4,#4 thread 2,0
#4,#4 thread 2,4
#4,#4 thread 2,2
libgomp: Number of places reduced from 8 to 1 because some places didn't
contain any usable logical CPUs
OMP_PROC_BIND='spread,master,close' OMP_PLACES='{0}:8'
Initial thread
#1 thread 0
#1 thread 3
#1 thread 2
#1 thread 1
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,0
#1,#2 thread 3,4
#1,#2 thread 3,3
#1,#2 thread 3,2
#1,#2 thread 3,1
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,0
#1,#4 thread 3,5
#1,#4 thread 3,4
#1,#4 thread 3,3
#1,#4 thread 3,2
#1,#4 thread 3,1
#2 thread 3
#2 thread 0
#2 thread 2
#2 thread 1
#2 thread 4
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,4
#2,#2 thread 3,3
#2,#2 thread 3,2
#2,#2 thread 3,1
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,0
#2,#4 thread 3,5
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,2
#2,#4 thread 3,1
#3 thread 1
#3 thread 2
#3 thread 0
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,0
#3,#2 thread 2,3
#3,#2 thread 2,2
#3,#2 thread 2,1
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,1
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,1
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#4 thread 2,0
#3,#4 thread 2,5
#3,#4 thread 2,4
#3,#4 thread 2,3
#3,#4 thread 2,2
#3,#4 thread 2,1
#4 thread 2
#4 thread 0
#4 thread 1
#4 thread 4
#4 thread 3
#4,#1 thread 2,0
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,1
#4,#2 thread 2,0
#4,#2 thread 2,3
#4,#2 thread 2,2
#4,#2 thread 2,1
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,1
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,1
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,3
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,1
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,0
#4,#4 thread 2,5
#4,#4 thread 2,4
#4,#4 thread 2,3
#4,#4 thread 2,2
#4,#4 thread 2,1
OMP_PROC_BIND='false'
Initial thread
#1 thread 0
#1 thread 2
#1 thread 3
#1 thread 1
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,0
#1,#2 thread 3,3
#1,#2 thread 3,2
#1,#2 thread 3,4
#1,#2 thread 3,1
#1,#2,#1 thread 3,3,1
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,3
#1,#3 thread 3,0
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#3 thread 3,3
#1,#4 thread 3,1
#1,#4 thread 3,2
#1,#4 thread 3,3
#1,#4 thread 3,0
#1,#4 thread 3,5
#1,#4 thread 3,4
#2 thread 0
#2 thread 2
#2 thread 4
#2 thread 3
#2 thread 1
#2,#1 thread 3,0
#2,#1 thread 3,1
#2,#1 thread 3,2
#2,#2 thread 3,1
#2,#2 thread 3,4
#2,#2 thread 3,3
#2,#2 thread 3,2
#2,#2 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,1
#2,#3 thread 3,0
#2,#3 thread 3,2
#2,#4 thread 3,1
#2,#4 thread 3,5
#2,#4 thread 3,3
#2,#4 thread 3,2
#2,#4 thread 3,4
#2,#4 thread 3,0
#3 thread 1
#3 thread 0
#3 thread 2
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,2
#3,#2 thread 2,3
#3,#2 thread 2,1
#3,#2 thread 2,0
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,1
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,4
#3,#2,#2 thread 2,3,1
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,3
#3,#3 thread 2,2
#3,#3 thread 2,3
#3,#3 thread 2,0
#3,#3 thread 2,1
#3,#4 thread 2,2
#3,#4 thread 2,0
#3,#4 thread 2,1
#3,#4 thread 2,3
#3,#4 thread 2,4
#3,#4 thread 2,5
#4 thread 3
#4 thread 4
#4 thread 0
#4 thread 1
#4 thread 2
#4,#1 thread 2,1
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,0
#4,#2 thread 2,1
#4,#2 thread 2,3
#4,#2 thread 2,2
#4,#2 thread 2,0
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,1
#4,#2,#1 thread 2,0,4
#4,#2,#2 thread 2,2,1
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,4
#4,#2,#3 thread 2,3,1
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,2
#4,#2,#3 thread 2,3,3
#4,#3 thread 2,2
#4,#3 thread 2,3
#4,#3 thread 2,1
#4,#3 thread 2,0
#4,#4 thread 2,1
#4,#4 thread 2,2
#4,#4 thread 2,3
#4,#4 thread 2,5
#4,#4 thread 2,4
#4,#4 thread 2,0
On 7 Oct, 2013, at 1:32 PM, jakub at gcc dot gnu.org <gcc-bugzilla@gcc.gnu.org>
wrote:
> http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
>
> --- Comment #20 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
> I'll commit the patch anyway, it is a step forward.
>
> Anyway, the way the testcase is written is that if you run it with
> OMP_PROC_BIND=false in the environment and OMP_PLACES unset, then it should
> fork and exec /proc/self/exe with various settings of those two environment
> variables.
> Can you perhaps see in the debugger what value has contig_cpucount variable at
> the start of main, and why it decided not to fork (or, has it failed to exec
> /proc/self/exe)?
>
> --
> You are receiving this mail because:
> You reported the bug.
--
Il est bon de suivre sa pente, pourvu que ce soit en montant.
A.G.
http://www.flickr.com/photos/vin60/1320965757/
>From gcc-bugs-return-431254-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org Mon Oct 07 12:16:46 2013
Return-Path: <gcc-bugs-return-431254-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org>
Delivered-To: listarch-gcc-bugs@gcc.gnu.org
Received: (qmail 30324 invoked by alias); 7 Oct 2013 12:16:46 -0000
Mailing-List: contact gcc-bugs-help@gcc.gnu.org; run by ezmlm
Precedence: bulk
List-Id: <gcc-bugs.gcc.gnu.org>
List-Archive: <http://gcc.gnu.org/ml/gcc-bugs/>
List-Post: <mailto:gcc-bugs@gcc.gnu.org>
List-Help: <mailto:gcc-bugs-help@gcc.gnu.org>
Sender: gcc-bugs-owner@gcc.gnu.org
Delivered-To: mailing list gcc-bugs@gcc.gnu.org
Received: (qmail 30278 invoked by uid 48); 7 Oct 2013 12:16:41 -0000
From: "jakub at gcc dot gnu.org" <gcc-bugzilla@gcc.gnu.org>
To: gcc-bugs@gcc.gnu.org
Subject: [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
Date: Mon, 07 Oct 2013 12:16:00 -0000
X-Bugzilla-Reason: CC
X-Bugzilla-Type: changed
X-Bugzilla-Watch-Reason: None
X-Bugzilla-Product: gcc
X-Bugzilla-Component: libgomp
X-Bugzilla-Version: 4.9.0
X-Bugzilla-Keywords:
X-Bugzilla-Severity: normal
X-Bugzilla-Who: jakub at gcc dot gnu.org
X-Bugzilla-Status: ASSIGNED
X-Bugzilla-Priority: P3
X-Bugzilla-Assigned-To: jakub at gcc dot gnu.org
X-Bugzilla-Target-Milestone: ---
X-Bugzilla-Flags:
X-Bugzilla-Changed-Fields:
Message-ID: <bug-58642-4-BYXxAQ8gqs@http.gcc.gnu.org/bugzilla/>
In-Reply-To: <bug-58642-4@http.gcc.gnu.org/bugzilla/>
References: <bug-58642-4@http.gcc.gnu.org/bugzilla/>
Content-Type: text/plain; charset="UTF-8"
Content-Transfer-Encoding: 7bit
X-Bugzilla-URL: http://gcc.gnu.org/bugzilla/
Auto-Submitted: auto-generated
MIME-Version: 1.0
X-SW-Source: 2013-10/txt/msg00398.txt.bz2
Content-length: 854
http://gcc.gnu.org/bugzilla/show_bug.cgi?idX642
--- Comment #23 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
Ah, right, obviously I meant
--- libgomp/testsuite/libgomp.c/affinity-1.c 2013-10-07 09:31:53.884695701
+0200
+++ libgomp/testsuite/libgomp.c/affinity-1.c 2013-10-07 14:09:52.475331358
+0200
@@ -178,7 +178,7 @@ main ()
int test_places = 0;
#ifdef DO_FORK
- if (env_places == NULL && contig_cpucount == 8 && test_false
+ if (env_places == NULL && contig_cpucount >= 8 && test_false
&& getenv ("GOMP_AFFINITY") == NULL)
{
int i, j, status;
(the other spot already correctly uses >= 8 - all the testcase cares about is
that the first 8 logical CPUs can be used for affinity).
That answers the not seeing fork case, but if it doesn't print any verified
lines even with that, there would be some other issue.
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (20 preceding siblings ...)
2013-10-07 12:07 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 12:43 ` vincenzo.innocente at cern dot ch
2013-10-07 13:22 ` vincenzo.innocente at cern dot ch
` (4 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 12:43 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #24 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
ok, modified to ">="
taskset -c 0-31 gdb ./affinity-1.exe
GNU gdb (GDB) Red Hat Enterprise Linux (7.2-60.el6_4.1)
(gdb) b
/home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:179
Breakpoint 1 at 0x400d5f: file
/home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c, line
179.
(gdb) run
Breakpoint 1, main () at
/home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:181
181 /home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:
No such file or directory.
in /home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c
Missing separate debuginfos, use: debuginfo-install
glibc-2.12-1.107.el6_4.4.x86_64
(gdb) print contig_cpucount
$1 = 32
and then spawn etc
but
taskset -c 24-31 gdb ./affinity-1.exe
Breakpoint 1, main () at
/home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:181
181 /home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c:
No such file or directory.
in /home/data/newsoft/gcc-gomp4/libgomp/testsuite/libgomp.c/affinity-1.c
Missing separate debuginfos, use: debuginfo-install
glibc-2.12-1.107.el6_4.4.x86_64
(gdb) print contig_cpucount
$1 = 0
I see anyhow where contig_cpucount is set.
up to you to generalize the test…
v.
On 7 Oct, 2013, at 2:16 PM, jakub at gcc dot gnu.org <gcc-bugzilla@gcc.gnu.org>
wrote:
> http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
>
> --- Comment #23 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
> Ah, right, obviously I meant
> --- libgomp/testsuite/libgomp.c/affinity-1.c 2013-10-07 09:31:53.884695701
> +0200
> +++ libgomp/testsuite/libgomp.c/affinity-1.c 2013-10-07 14:09:52.475331358
> +0200
> @@ -178,7 +178,7 @@ main ()
> int test_places = 0;
>
> #ifdef DO_FORK
> - if (env_places == NULL && contig_cpucount == 8 && test_false
> + if (env_places == NULL && contig_cpucount >= 8 && test_false
> && getenv ("GOMP_AFFINITY") == NULL)
> {
> int i, j, status;
> (the other spot already correctly uses >= 8 - all the testcase cares about is
> that the first 8 logical CPUs can be used for affinity).
> That answers the not seeing fork case, but if it doesn't print any verified
> lines even with that, there would be some other issue.
>
> --
> You are receiving this mail because:
> You reported the bug.
--
Il est bon de suivre sa pente, pourvu que ce soit en montant.
A.G.
http://www.flickr.com/photos/vin60/1320965757/
>From gcc-bugs-return-431258-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org Mon Oct 07 13:02:25 2013
Return-Path: <gcc-bugs-return-431258-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org>
Delivered-To: listarch-gcc-bugs@gcc.gnu.org
Received: (qmail 773 invoked by alias); 7 Oct 2013 13:02:24 -0000
Mailing-List: contact gcc-bugs-help@gcc.gnu.org; run by ezmlm
Precedence: bulk
List-Id: <gcc-bugs.gcc.gnu.org>
List-Archive: <http://gcc.gnu.org/ml/gcc-bugs/>
List-Post: <mailto:gcc-bugs@gcc.gnu.org>
List-Help: <mailto:gcc-bugs-help@gcc.gnu.org>
Sender: gcc-bugs-owner@gcc.gnu.org
Delivered-To: mailing list gcc-bugs@gcc.gnu.org
Received: (qmail 737 invoked by uid 48); 7 Oct 2013 13:02:22 -0000
From: "jakub at gcc dot gnu.org" <gcc-bugzilla@gcc.gnu.org>
To: gcc-bugs@gcc.gnu.org
Subject: [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
Date: Mon, 07 Oct 2013 13:02:00 -0000
X-Bugzilla-Reason: CC
X-Bugzilla-Type: changed
X-Bugzilla-Watch-Reason: None
X-Bugzilla-Product: gcc
X-Bugzilla-Component: libgomp
X-Bugzilla-Version: 4.9.0
X-Bugzilla-Keywords:
X-Bugzilla-Severity: normal
X-Bugzilla-Who: jakub at gcc dot gnu.org
X-Bugzilla-Status: ASSIGNED
X-Bugzilla-Priority: P3
X-Bugzilla-Assigned-To: jakub at gcc dot gnu.org
X-Bugzilla-Target-Milestone: ---
X-Bugzilla-Flags:
X-Bugzilla-Changed-Fields:
Message-ID: <bug-58642-4-KrBY9KzspN@http.gcc.gnu.org/bugzilla/>
In-Reply-To: <bug-58642-4@http.gcc.gnu.org/bugzilla/>
References: <bug-58642-4@http.gcc.gnu.org/bugzilla/>
Content-Type: text/plain; charset="UTF-8"
Content-Transfer-Encoding: 7bit
X-Bugzilla-URL: http://gcc.gnu.org/bugzilla/
Auto-Submitted: auto-generated
MIME-Version: 1.0
X-SW-Source: 2013-10/txt/msg00402.txt.bz2
Content-length: 356
http://gcc.gnu.org/bugzilla/show_bug.cgi?idX642
--- Comment #25 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
It is fine if the testcase doesn't fork and doesn't verify for taskset -c
24-31, that would be too hard to support, the testcase doesn't fail because of
that.
But, do you get the ", verified" strings in the lines for taskset -c 0-31 run?
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (21 preceding siblings ...)
2013-10-07 12:43 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 13:22 ` vincenzo.innocente at cern dot ch
2013-10-07 17:04 ` jakub at gcc dot gnu.org
` (3 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-07 13:22 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #26 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
On 7 Oct, 2013, at 3:02 PM, jakub at gcc dot gnu.org <gcc-bugzilla@gcc.gnu.org>
wrote:
> http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
>
> --- Comment #25 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
> It is fine if the testcase doesn't fork and doesn't verify for taskset -c
> 24-31, that would be too hard to support, the testcase doesn't fail because of
> that.
> But, do you get the ", verified" strings in the lines for taskset -c 0-31 run?
>
on the build machine yes
echo $OMP_PROC_BIND
false
[innocent@vinavx0 testsuite]$ ./affinity-1.exe | grep veri | wc
1065 7445 44193
on the XEON
nope
echo $OMP_PROC_BIND
false
[innocent@olsnba04 parallel]$ ./affinity-1.exe | grep veri
libgomp: Number of places reduced from 5 to 1 because some places didn't
contain any usable logical CPUs
libgomp: None of the places contain usable logical CPUs
libgomp: Invalid value for environment variable OMP_PLACES
libgomp: Number of places reduced from 3 to 1 because some places didn't
contain any usable logical CPUs
libgomp: None of the places contain usable logical CPUs
libgomp: Invalid value for environment variable OMP_PLACES
libgomp: Number of places reduced from 8 to 1 because some places didn't
contain any usable logical CPUs
libgomp: Number of places reduced from 5 to 1 because some places didn't
contain any usable logical CPUs
libgomp: None of the places contain usable logical CPUs
libgomp: Invalid value for environment variable OMP_PLACES
libgomp: Number of places reduced from 3 to 1 because some places didn't
contain any usable logical CPUs
libgomp: None of the places contain usable logical CPUs
libgomp: Invalid value for environment variable OMP_PLACES
libgomp: Number of places reduced from 8 to 1 because some places didn't
contain any usable logical CPUs
same for
taskset -c 0-8 ./affinity-1.exe | grep veri
> --
> You are receiving this mail because:
> You reported the bug.
--
Il est bon de suivre sa pente, pourvu que ce soit en montant.
A.G.
http://www.flickr.com/photos/vin60/1320965757/
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (22 preceding siblings ...)
2013-10-07 13:22 ` vincenzo.innocente at cern dot ch
@ 2013-10-07 17:04 ` jakub at gcc dot gnu.org
2013-10-08 6:40 ` vincenzo.innocente at cern dot ch
` (2 subsequent siblings)
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-07 17:04 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #27 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
(In reply to vincenzo Innocente from comment #26)
> [innocent@olsnba04 parallel]$ ./affinity-1.exe | grep veri
>
> libgomp: Number of places reduced from 5 to 1 because some places didn't
> contain any usable logical CPUs
>
> libgomp: None of the places contain usable logical CPUs
>
> libgomp: Invalid value for environment variable OMP_PLACES
Ugh, none of these look expected. Can you cut'n'paste the
OMP_PROC_BIND=... OMP_PLACES=...
line from before some of these errors and see if you can
reproduce it with running ./affinity-1.exe with those two env vars?
Can you strace | grep affinity it?
The == 8 to >= 8 change is already in the gomp-4_0-branch BTW.
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (23 preceding siblings ...)
2013-10-07 17:04 ` jakub at gcc dot gnu.org
@ 2013-10-08 6:40 ` vincenzo.innocente at cern dot ch
2013-10-08 7:22 ` vincenzo.innocente at cern dot ch
2013-10-11 10:40 ` jakub at gcc dot gnu.org
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-08 6:40 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #28 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
updated to the new revision
gcc version 4.9.0 20131007 (experimental) [gomp-4_0-branch revision 203250]
(GCC)
[innocent@olsnba04 parallel]$ setenv OMP_PROC_BIND 'spread,master,close';
setenv OMP_PLACES '{0}:8'
[innocent@olsnba04 parallel]$ printenv | grep OMP
OMP_PROC_BIND=spread,master,close
OMP_PLACES={0}:8
[innocent@olsnba04 parallel]$ strace ./affinity-1.exe | & grep affin
execve("./affinity-1.exe", ["./affinity-1.exe"], [/* 61 vars */]) = 0
sched_getaffinity(109733, 8, 0x1dc8010) = -1 EINVAL (Invalid argument)
sched_getaffinity(109733, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
sched_getaffinity(109733, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
sched_setaffinity(109733, 8, { 1 }) = 0
sched_getaffinity(109733, 8, 0x7fff71425940) = -1 EINVAL (Invalid argument)
sched_setaffinity(109734, 8, { 4 }) = 0
sched_setaffinity(109735, 8, { 10 }) = 0
sched_setaffinity(109736, 8, { 40 }) = 0
sched_getaffinity(109733, 8, 0x7fff714258c0) = -1 EINVAL (Invalid argument)
sched_setaffinity(109755, 8, { 80 }) = 0
sched_getaffinity(109733, 8, 0x7fff714258b0) = -1 EINVAL (Invalid argument)
sched_setaffinity(109770, 8, { 1 }) = 0
sched_setaffinity(109771, 8, { 1 }) = 0
sched_getaffinity(109733, 8, 0x7fff714258c0) = -1 EINVAL (Invalid argument)
sched_setaffinity(109794, 8, { 2 }) = 0
sched_setaffinity(109795, 8, { 4 }) = 0
sched_setaffinity(109796, 8, { 8 }) = 0
sched_setaffinity(109797, 8, { 10 }) = 0
sched_getaffinity(109733, 8, 0x7fff714258b0) = -1 EINVAL (Invalid argument)
[innocent@olsnba04 parallel]$ ./affinity-1.exe
OMP_PROC_BIND='spread,master,close' OMP_PLACES='{0}:8'
Initial thread
#1 thread 0
#1 thread 2
#1 thread 1
#1 thread 3
#1,#1 thread 3,0
#1,#1 thread 3,2
#1,#1 thread 3,1
#1,#2 thread 3,3
#1,#2 thread 3,0
#1,#2 thread 3,2
#1,#2 thread 3,4
#1,#2 thread 3,1
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#3 thread 3,1
#1,#4 thread 3,5
#1,#4 thread 3,0
#1,#4 thread 3,4
#1,#4 thread 3,2
#1,#4 thread 3,3
#1,#4 thread 3,1
#2 thread 0
#2 thread 3
#2 thread 1
#2 thread 2
#2 thread 4
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#1 thread 3,1
#2,#2 thread 3,0
#2,#2 thread 3,4
#2,#2 thread 3,3
#2,#2 thread 3,2
#2,#2 thread 3,1
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#3 thread 3,2
#2,#3 thread 3,1
#2,#4 thread 3,0
#2,#4 thread 3,5
#2,#4 thread 3,4
#2,#4 thread 3,3
#2,#4 thread 3,2
#2,#4 thread 3,1
#3 thread 0
#3 thread 2
#3 thread 1
#3,#1 thread 2,0
#3,#1 thread 2,3
#3,#1 thread 2,2
#3,#1 thread 2,1
#3,#2 thread 2,2
#3,#2 thread 2,1
#3,#2 thread 2,0
#3,#2 thread 2,3
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,1
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,1
#3,#3 thread 2,0
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#3 thread 2,1
#3,#4 thread 2,5
#3,#4 thread 2,1
#3,#4 thread 2,0
#3,#4 thread 2,2
#3,#4 thread 2,3
#3,#4 thread 2,4
#4 thread 1
#4 thread 2
#4 thread 3
#4 thread 4
#4 thread 0
#4,#1 thread 2,0
#4,#1 thread 2,3
#4,#1 thread 2,2
#4,#1 thread 2,1
#4,#2 thread 2,1
#4,#2 thread 2,3
#4,#2 thread 2,2
#4,#2 thread 2,0
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,4
#4,#2,#1 thread 2,0,1
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,3
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,2
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,1
#4,#2,#3 thread 2,3,3
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,1
#4,#2,#3 thread 2,3,2
#4,#3 thread 2,0
#4,#3 thread 2,3
#4,#3 thread 2,2
#4,#3 thread 2,1
#4,#4 thread 2,2
#4,#4 thread 2,5
#4,#4 thread 2,4
#4,#4 thread 2,0
#4,#4 thread 2,1
#4,#4 thread 2,3
[innocent@olsnba04 parallel]$ setenv OMP_PROC_BIND 'spread,master,close';
setenv OMP_PLACES '{7,6}:2:-3'
[innocent@olsnba04 parallel]$ printenv | grep OMP
OMP_PROC_BIND=spread,master,close
OMP_PLACES={7,6}:2:-3
strace ./affinity-1.exe |& grep affin
execve("./affinity-1.exe", ["./affinity-1.exe"], [/* 61 vars */]) = 0
sched_getaffinity(109640, 8, 0x24e9010) = -1 EINVAL (Invalid argument)
sched_getaffinity(109640, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
sched_getaffinity(109640, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
sched_setaffinity(109640, 8, { c0 }) = 0
sched_getaffinity(109640, 8, 0x7fffaeaeda40) = -1 EINVAL (Invalid argument)
sched_setaffinity(109641, 8, { c0 }) = 0
sched_setaffinity(109642, 8, { 18 }) = 0
sched_setaffinity(109643, 8, { 18 }) = 0
sched_getaffinity(109640, 8, 0x7fffaeaed9c0) = -1 EINVAL (Invalid argument)
sched_setaffinity(109662, 8, { c0 }) = 0
sched_getaffinity(109640, 8, 0x7fffaeaed9b0) = -1 EINVAL (Invalid argument)
sched_getaffinity(109640, 8, 0x7fffaeaed9c0) = -1 EINVAL (Invalid argument)
sched_setaffinity(109699, 8, { 18 }) = 0
sched_setaffinity(109700, 8, { 18 }) = 0
sched_getaffinity(109640, 8, 0x7fffaeaed9b0) = -1 EINVAL (Invalid argument)
[innocent@olsnba04 parallel]$ ./affinity-1.exe
OMP_PROC_BIND='spread,master,close' OMP_PLACES='{7,6}:2:-3'
Initial thread
#1 thread 0
#1 thread 3
#1 thread 1
#1 thread 2
#1,#1 thread 3,1
#1,#1 thread 3,2
#1,#1 thread 3,0
#1,#2 thread 3,2
#1,#2 thread 3,3
#1,#2 thread 3,0
#1,#2 thread 3,1
#1,#2 thread 3,4
#1,#2,#1 thread 3,3,3
#1,#2,#1 thread 3,3,0
#1,#2,#1 thread 3,3,2
#1,#2,#1 thread 3,3,4
#1,#2,#1 thread 3,3,1
#1,#3 thread 3,1
#1,#3 thread 3,0
#1,#3 thread 3,3
#1,#3 thread 3,2
#1,#4 thread 3,1
#1,#4 thread 3,0
#1,#4 thread 3,5
#1,#4 thread 3,4
#1,#4 thread 3,3
#1,#4 thread 3,2
#2 thread 2
#2 thread 0
#2 thread 3
#2 thread 1
#2 thread 4
#2,#1 thread 3,1
#2,#1 thread 3,0
#2,#1 thread 3,2
#2,#2 thread 3,0
#2,#2 thread 3,2
#2,#2 thread 3,3
#2,#2 thread 3,1
#2,#2 thread 3,4
#2,#3 thread 3,1
#2,#3 thread 3,2
#2,#3 thread 3,0
#2,#3 thread 3,3
#2,#4 thread 3,0
#2,#4 thread 3,3
#2,#4 thread 3,4
#2,#4 thread 3,1
#2,#4 thread 3,5
#2,#4 thread 3,2
#3 thread 0
#3 thread 2
#3 thread 1
#3,#1 thread 2,2
#3,#1 thread 2,0
#3,#1 thread 2,1
#3,#1 thread 2,3
#3,#2 thread 2,0
#3,#2 thread 2,1
#3,#2 thread 2,3
#3,#2 thread 2,2
#3,#2,#1 thread 2,0,3
#3,#2,#1 thread 2,0,0
#3,#2,#1 thread 2,0,2
#3,#2,#1 thread 2,0,4
#3,#2,#1 thread 2,0,1
#3,#2,#2 thread 2,3,4
#3,#2,#2 thread 2,3,0
#3,#2,#2 thread 2,3,2
#3,#2,#2 thread 2,3,3
#3,#2,#2 thread 2,3,1
#3,#3 thread 2,0
#3,#3 thread 2,1
#3,#3 thread 2,3
#3,#3 thread 2,2
#3,#4 thread 2,3
#3,#4 thread 2,0
#3,#4 thread 2,1
#3,#4 thread 2,4
#3,#4 thread 2,5
#3,#4 thread 2,2
#4 thread 1
#4 thread 3
#4 thread 4
#4 thread 2
#4 thread 0
#4,#1 thread 2,1
#4,#1 thread 2,0
#4,#1 thread 2,2
#4,#1 thread 2,3
#4,#2 thread 2,2
#4,#2 thread 2,1
#4,#2 thread 2,3
#4,#2 thread 2,0
#4,#2,#1 thread 2,0,3
#4,#2,#1 thread 2,0,0
#4,#2,#1 thread 2,0,2
#4,#2,#1 thread 2,0,1
#4,#2,#1 thread 2,0,4
#4,#2,#2 thread 2,2,1
#4,#2,#2 thread 2,2,0
#4,#2,#2 thread 2,2,3
#4,#2,#2 thread 2,2,4
#4,#2,#2 thread 2,2,2
#4,#2,#3 thread 2,3,4
#4,#2,#3 thread 2,3,0
#4,#2,#3 thread 2,3,3
#4,#2,#3 thread 2,3,1
#4,#2,#3 thread 2,3,2
#4,#3 thread 2,1
#4,#3 thread 2,0
#4,#3 thread 2,2
#4,#3 thread 2,3
#4,#4 thread 2,2
#4,#4 thread 2,3
#4,#4 thread 2,0
#4,#4 thread 2,5
#4,#4 thread 2,1
#4,#4 thread 2,4
[innocent@olsnba04 parallel]$
>>
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (24 preceding siblings ...)
2013-10-08 6:40 ` vincenzo.innocente at cern dot ch
@ 2013-10-08 7:22 ` vincenzo.innocente at cern dot ch
2013-10-11 10:40 ` jakub at gcc dot gnu.org
26 siblings, 0 replies; 28+ messages in thread
From: vincenzo.innocente at cern dot ch @ 2013-10-08 7:22 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
--- Comment #30 from vincenzo Innocente <vincenzo.innocente at cern dot ch> ---
better: as usual nastier bugs are in the tests!
[innocent@olsnba04 parallel]$ strace ./affinity-1.exe | & grep affin
execve("./affinity-1.exe", ["./affinity-1.exe"], [/* 61 vars */]) = 0
sched_getaffinity(110481, 8, 0x7b8010) = -1 EINVAL (Invalid argument)
sched_getaffinity(110481, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
sched_getaffinity(110481, 128, { ffffffff, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0, 0, 0 }) = 128
sched_setaffinity(110481, 8, { 1 }) = 0
sched_getaffinity(110481, 128, { 1, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0 }) = 128
sched_setaffinity(110482, 8, { 4 }) = 0
sched_setaffinity(110483, 8, { 10 }) = 0
sched_setaffinity(110484, 8, { 40 }) = 0
sched_getaffinity(110481, 128, { 1, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0 }) = 128
sched_setaffinity(110503, 8, { 80 }) = 0
sched_getaffinity(110481, 128, { 1, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0 }) = 128
sched_setaffinity(110518, 8, { 1 }) = 0
sched_setaffinity(110519, 8, { 1 }) = 0
sched_getaffinity(110481, 128, { 1, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0 }) = 128
sched_setaffinity(110542, 8, { 2 }) = 0
sched_setaffinity(110543, 8, { 4 }) = 0
sched_setaffinity(110544, 8, { 8 }) = 0
sched_setaffinity(110545, 8, { 10 }) = 0
sched_getaffinity(110481, 128, { 1, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0,
0 }) = 128
[innocent@olsnba04 parallel]$ ./affinity-1.exe
OMP_PROC_BIND='spread,master,close' OMP_PLACES='{0}:8'
Initial thread bound to {0}, verified
#1 thread 0 bound to {0}, verified
#1 thread 1 bound to {2}, verified
#1 thread 2 bound to {4}, verified
#1 thread 3 bound to {6}, verified
#1,#1 thread 3,0 bound to {6}, verified
#1,#1 thread 3,2 bound to {6}, verified
#1,#1 thread 3,1 bound to {6}, verified
#1,#2 thread 3,0 bound to {6}, verified
#1,#2 thread 3,3 bound to {7}, verified
#1,#2 thread 3,4 bound to {6}, verified
#1,#2 thread 3,2 bound to {7}, verified
#1,#2 thread 3,1 bound to {6}, verified
#1,#2,#1 thread 3,3,0 bound to {7}, verified
#1,#2,#1 thread 3,3,4 bound to {7}, verified
#1,#2,#1 thread 3,3,3 bound to {7}, verified
#1,#2,#1 thread 3,3,2 bound to {7}, verified
#1,#2,#1 thread 3,3,1 bound to {7}, verified
#1,#3 thread 3,0 bound to {6}, verified
#1,#3 thread 3,3 bound to {6}, verified
#1,#3 thread 3,2 bound to {6}, verified
#1,#3 thread 3,1 bound to {6}, verified
#1,#4 thread 3,4 bound to {7}, verified
#1,#4 thread 3,0 bound to {6}, verified
#1,#4 thread 3,3 bound to {7}, verified
#1,#4 thread 3,2 bound to {6}, verified
#1,#4 thread 3,5 bound to {7}, verified
#1,#4 thread 3,1 bound to {6}, verified
#2 thread 0 bound to {0}, verified
#2 thread 1 bound to {2}, verified
#2 thread 3 bound to {6}, verified
#2 thread 4 bound to {7}, verified
#2 thread 2 bound to {4}, verified
#2,#1 thread 3,0 bound to {6}, verified
#2,#1 thread 3,2 bound to {6}, verified
#2,#1 thread 3,1 bound to {6}, verified
#2,#2 thread 3,0 bound to {6}, verified
#2,#2 thread 3,4 bound to {6}, verified
#2,#2 thread 3,3 bound to {6}, verified
#2,#2 thread 3,2 bound to {6}, verified
#2,#2 thread 3,1 bound to {6}, verified
#2,#3 thread 3,0 bound to {6}, verified
#2,#3 thread 3,3 bound to {6}, verified
#2,#3 thread 3,2 bound to {6}, verified
#2,#3 thread 3,1 bound to {6}, verified
#2,#4 thread 3,0 bound to {6}, verified
#2,#4 thread 3,5 bound to {6}, verified
#2,#4 thread 3,4 bound to {6}, verified
#2,#4 thread 3,3 bound to {6}, verified
#2,#4 thread 3,2 bound to {6}, verified
#2,#4 thread 3,1 bound to {6}, verified
#3 thread 0 bound to {0}, verified
#3 thread 2 bound to {0}, verified
#3 thread 1 bound to {0}, verified
#3,#1 thread 2,0 bound to {0}, verified
#3,#1 thread 2,3 bound to {0}, verified
#3,#1 thread 2,2 bound to {0}, verified
#3,#1 thread 2,1 bound to {0}, verified
#3,#2 thread 2,2 bound to {4}, verified
#3,#2 thread 2,1 bound to {2}, verified
#3,#2 thread 2,0 bound to {0}, verified
#3,#2 thread 2,3 bound to {6}, verified
#3,#2,#1 thread 2,0,1 bound to {0}, verified
#3,#2,#1 thread 2,0,0 bound to {0}, verified
#3,#2,#1 thread 2,0,3 bound to {1}, verified
#3,#2,#1 thread 2,0,4 bound to {0}, verified
#3,#2,#1 thread 2,0,2 bound to {1}, verified
#3,#2,#2 thread 2,3,0 bound to {6}, verified
#3,#2,#2 thread 2,3,3 bound to {7}, verified
#3,#2,#2 thread 2,3,2 bound to {7}, verified
#3,#2,#2 thread 2,3,4 bound to {6}, verified
#3,#2,#2 thread 2,3,1 bound to {6}, verified
#3,#3 thread 2,0 bound to {0}, verified
#3,#3 thread 2,3 bound to {0}, verified
#3,#3 thread 2,2 bound to {0}, verified
#3,#3 thread 2,1 bound to {0}, verified
#3,#4 thread 2,1 bound to {1}, verified
#3,#4 thread 2,5 bound to {5}, verified
#3,#4 thread 2,3 bound to {3}, verified
#3,#4 thread 2,0 bound to {0}, verified
#3,#4 thread 2,2 bound to {2}, verified
#3,#4 thread 2,4 bound to {4}, verified
#4 thread 1 bound to {1}, verified
#4 thread 2 bound to {2}, verified
#4 thread 3 bound to {3}, verified
#4 thread 4 bound to {4}, verified
#4 thread 0 bound to {0}, verified
#4,#1 thread 2,0 bound to {2}, verified
#4,#1 thread 2,3 bound to {2}, verified
#4,#1 thread 2,2 bound to {2}, verified
#4,#1 thread 2,1 bound to {2}, verified
#4,#2 thread 2,1 bound to {4}, verified
#4,#2 thread 2,3 bound to {0}, verified
#4,#2 thread 2,2 bound to {6}, verified
#4,#2 thread 2,0 bound to {2}, verified
#4,#2,#1 thread 2,0,0 bound to {2}, verified
#4,#2,#1 thread 2,0,3 bound to {3}, verified
#4,#2,#1 thread 2,0,2 bound to {3}, verified
#4,#2,#1 thread 2,0,4 bound to {2}, verified
#4,#2,#1 thread 2,0,1 bound to {2}, verified
#4,#2,#2 thread 2,2,3 bound to {7}, verified
#4,#2,#2 thread 2,2,2 bound to {7}, verified
#4,#2,#2 thread 2,2,4 bound to {6}, verified
#4,#2,#2 thread 2,2,1 bound to {6}, verified
#4,#2,#2 thread 2,2,0 bound to {6}, verified
#4,#2,#3 thread 2,3,2 bound to {1}, verified
#4,#2,#3 thread 2,3,0 bound to {0}, verified
#4,#2,#3 thread 2,3,4 bound to {0}, verified
#4,#2,#3 thread 2,3,1 bound to {0}, verified
#4,#2,#3 thread 2,3,3 bound to {1}, verified
#4,#3 thread 2,0 bound to {2}, verified
#4,#3 thread 2,3 bound to {2}, verified
#4,#3 thread 2,2 bound to {2}, verified
#4,#3 thread 2,1 bound to {2}, verified
#4,#4 thread 2,1 bound to {3}, verified
#4,#4 thread 2,2 bound to {4}, verified
#4,#4 thread 2,5 bound to {7}, verified
#4,#4 thread 2,4 bound to {6}, verified
#4,#4 thread 2,0 bound to {2}, verified
#4,#4 thread 2,3 bound to {5}, verified
./affinity-1.exe | grep verified | wc
1065 7445 44193
taskset -c 0-15 ./affinity-1.exe | grep gomp | wc
0 0 0
[innocent@olsnba04 parallel]$
> http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
>
> --- Comment #29 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
> Created attachment 30967
> --> http://gcc.gnu.org/bugzilla/attachment.cgi?id=30967&action=edit
> Y
>
> Ah, thanks, I can see where the failing sched_getaffinity calls are coming
> from, hopefully this patch should fix that.
>
> That doesn't explain the libgomp errors you were getting though (if you can
> still reproduce them).
> To track that perhaps we could instrument libgomp to tell us more details.
>
> --
> You are receiving this mail because:
> You reported the bug.
--
Il est bon de suivre sa pente, pourvu que ce soit en montant.
A.G.
http://www.flickr.com/photos/vin60/1320965757/
^ permalink raw reply [flat|nested] 28+ messages in thread
* [Bug libgomp/58642] gomp regression: not "honoring" anymore task set and numactl
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
` (25 preceding siblings ...)
2013-10-08 7:22 ` vincenzo.innocente at cern dot ch
@ 2013-10-11 10:40 ` jakub at gcc dot gnu.org
26 siblings, 0 replies; 28+ messages in thread
From: jakub at gcc dot gnu.org @ 2013-10-11 10:40 UTC (permalink / raw)
To: gcc-bugs
http://gcc.gnu.org/bugzilla/show_bug.cgi?id=58642
Jakub Jelinek <jakub at gcc dot gnu.org> changed:
What |Removed |Added
----------------------------------------------------------------------------
Status|ASSIGNED |RESOLVED
Resolution|--- |FIXED
--- Comment #31 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
Fixed on the trunk now (gomp4 branch merged into trunk).
^ permalink raw reply [flat|nested] 28+ messages in thread
end of thread, other threads:[~2013-10-11 10:40 UTC | newest]
Thread overview: 28+ messages (download: mbox.gz / follow: Atom feed)
-- links below jump to the message on this page --
2013-10-06 13:42 [Bug libgomp/58642] New: gomp regression: not "honoring" anymore task set and numactl vincenzo.innocente at cern dot ch
2013-10-06 13:56 ` [Bug libgomp/58642] " jakub at gcc dot gnu.org
2013-10-06 14:05 ` jakub at gcc dot gnu.org
2013-10-06 14:38 ` vincenzo.innocente at cern dot ch
2013-10-06 15:15 ` vincenzo.innocente at cern dot ch
2013-10-06 18:02 ` jakub at gcc dot gnu.org
2013-10-06 19:31 ` jakub at gcc dot gnu.org
2013-10-07 6:49 ` vincenzo.innocente at cern dot ch
2013-10-07 6:53 ` vincenzo.innocente at cern dot ch
2013-10-07 7:47 ` jakub at gcc dot gnu.org
2013-10-07 7:58 ` vincenzo.innocente at cern dot ch
2013-10-07 8:04 ` jakub at gcc dot gnu.org
2013-10-07 8:06 ` jakub at gcc dot gnu.org
2013-10-07 8:08 ` vincenzo.innocente at cern dot ch
2013-10-07 8:12 ` vincenzo.innocente at cern dot ch
2013-10-07 10:14 ` vincenzo.innocente at cern dot ch
2013-10-07 10:28 ` jakub at gcc dot gnu.org
2013-10-07 11:03 ` vincenzo.innocente at cern dot ch
2013-10-07 11:06 ` vincenzo.innocente at cern dot ch
2013-10-07 11:32 ` jakub at gcc dot gnu.org
2013-10-07 11:39 ` jakub at gcc dot gnu.org
2013-10-07 12:07 ` vincenzo.innocente at cern dot ch
2013-10-07 12:43 ` vincenzo.innocente at cern dot ch
2013-10-07 13:22 ` vincenzo.innocente at cern dot ch
2013-10-07 17:04 ` jakub at gcc dot gnu.org
2013-10-08 6:40 ` vincenzo.innocente at cern dot ch
2013-10-08 7:22 ` vincenzo.innocente at cern dot ch
2013-10-11 10:40 ` jakub at gcc dot gnu.org
This is a public inbox, see mirroring instructions
for how to clone and mirror all data and code used for this inbox;
as well as URLs for read-only IMAP folder(s) and NNTP newsgroup(s).