Commit Graph

637 Commits

Author SHA1 Message Date
matt
6cb6b78422 Deal with MKPICLIB=no fallout 2013-02-14 00:53:30 +00:00
matt
4b5bef3f0b If compiling with apcs-gnu or atpcs ABIs, supply -mabi=gnu to gas. 2013-02-05 19:29:13 +00:00
matt
6984b4168c Backout setting of UNWIND_H 2013-02-05 08:28:15 +00:00
matt
cae58222cc Don't include t-arm-elf since it just provides stuff which netbsd already has. 2013-02-05 03:02:10 +00:00
matt
912dc5c278 updated mknative gcc bits for earmhf 2013-02-05 02:57:54 +00:00
matt
db87bbedd6 Rerun mknative for earm and earmhf for gas changes. 2013-02-04 22:50:12 +00:00
matt
13994434d1 Move arm-*-netbsdelf-*eabi* to before arm-*-eabi* so it matches properly.
Add arm-*-netbsdelf-*eabihf* which has a VFP V2 by default.
Rename armnetbsdeabi*.h to armnbsdeabi*.h to be consistent with other nbsd
files.
2013-02-04 22:38:07 +00:00
matt
5b98504a16 Add a match for arm*--netbsdelf-eabi* and default that EABI with a VFP FPU
and ARCH_ARM_V5TEJ cpu.
2013-02-04 18:42:30 +00:00
matt
a34eb5c25e Default to EABI5. Don't supply -meabi= to as. switch back unwind-arm.h
nuke unwind-netbsd.h
2013-02-04 18:41:18 +00:00
matt
442c893d77 mknative gdb for earmhf 2013-02-04 03:29:45 +00:00
matt
f07f4bab6c gcc mknative for earmhf 2013-02-04 01:22:14 +00:00
matt
15d372dbba mknative for earmhf 2013-02-03 05:34:50 +00:00
matt
c5775ada06 earmhf mknative for libgcc 2013-02-03 02:01:19 +00:00
matt
eeb9da25fc Use MACHINE_CPU for arm instead of MACHINE_ARCH 2013-02-03 01:59:55 +00:00
matt
2e93500115 binutils mknative for earmhf 2013-02-03 01:58:13 +00:00
matt
d6f7d83d82 Can't use TARGET_AAPCS_BASED since it's not setup by the time
SUBTARGET_CPU_DEFAULT is invoked so use ARM_DEFAULT_ABI instead).
2013-02-02 05:04:25 +00:00
matt
c510eba682 Add a unwind-netbsd.h which will include the proper unwind.h file depending
on __ARM_EABI__.  This allow gcc to build libgcc for both ABIs properly since
they both different unwind.h.
2013-01-31 07:11:08 +00:00
matt
8355d788c7 Cleanup arm--netbsdelf-*eabi* 2013-01-31 06:53:21 +00:00
matt
8728f6bef4 Define size_t, ptrdiff_t, and wchar_t to what NetBSD/arm wants instead of the
stupid values chosen for AAPCS.
2013-01-31 06:52:16 +00:00
matt
58ca788453 Make GCC define __ARM_PCS and __ARM_PCS_VFP as defined by the ARM C Language
Extentions (clang already defines them):
__ARM_PCS is defined to 1 if the default procedure calling standard for
the translation unit conforms to the "base PCS" defined in [AAPCS].
__ARM_PCS_VFP is defined to 1 if the default is to pass floating-point
parameters in hardware floating-point registers using the "VFP variant PCS"
defined in [AAPCS].
2013-01-25 08:31:43 +00:00
christos
62b158cdce Apply GCC/35998 from FreeBSD http://svnweb.freebsd.org/changeset/base/245024
gcc: avoid generating negative values to DW_AT_byte_size.

There is a bug in gcc (GCC/35998) where dwarf reports
sizes of unsigned -1 (0xffffffff).

On NetBSD this generated a faulty CTF entry which then
caused a segfault in ctfmerge. The issue was worked
around in NetBSD's Dtrace but since the issue originated
in gcc, it seems reasonable to fix it here.

Thanks to Christoph Mallon for pointing out a correct fix.
2013-01-17 19:10:56 +00:00
pooka
9cc8b77e83 ... but make sure to unset empty before it's used as an empty variable. 2013-01-14 16:00:49 +00:00
pooka
cdaf970fbf Make this work with xpg4/sh where "for x in;" is an error. 2013-01-14 15:50:18 +00:00
matt
6093c05ac7 Add missing % to SUBTARGET_ASM_FLOAT_SPEC
If compiling for AAPCS, default to a TARGET_CPU_arm926ejs (armv5te)
If linking for AAPCS, use the right linker emulation.
2013-01-11 13:58:40 +00:00
dsl
8a7a69a21d amd64's machine/reg now includes fpu.h (to define 'struct fxsave64)
so no need to include signal.h here - which shouldn't result in
the definitions in fpu.h being included anyway.
2013-01-02 18:44:46 +00:00
dsl
f5cd40cc56 No need to check both TARGET_64BIT and ix86_preferred_stack_boundary >= 64,
if the former is true the latter is also true.
2012-12-30 20:16:58 +00:00
dsl
c18b7a38ac If -march=native is specified, only enable AVX if the processor supports
it and the OS has enabled XGETBV for application use.
It might need to also check XCR0[2] (having executed XGETBV) to check that
  the kernel actually supports saving the YMM registers, but I suspect the
  kernel might defer setting that until the first fault.
See vol 1 section 13.5 of the Intel SDM (intel_x86_325462.pdf).
Fixes toolchain/45673
2012-12-30 16:13:57 +00:00
martin
5e4c896995 ia64 mknative results for gcc and binutils 2012-12-27 20:32:41 +00:00
martin
7657b23ac4 We do not have a native libunwind (yet) - so reuse the Linux stuff on ia64
for now.
2012-12-20 07:12:26 +00:00
martin
7b7b3a04a8 Avoid duplicate definition of __enable_execute_stack in libgcc (copied from
the rs6000 netbsd.h)
2012-12-19 16:57:21 +00:00
skrll
1b59d35cc3 Remove G_CONFIGDIR from .PATH as nothing defines it (anymore)
Add the paths from G_LIB2ADDEH to .PATH (for ia64)
2012-12-16 15:32:38 +00:00
christos
cfd7c4b684 XXX: Use earm for earmeb 2012-12-08 02:35:06 +00:00
christos
decff94806 fix inconsistencies in EABI decls. 2012-12-08 01:38:26 +00:00
christos
06c8deb857 If we did not include a specific arch file G_UNWIND_H will not be defined.
Perhaps it is better to error out in that case?
2012-12-07 15:38:04 +00:00
matt
1ca4d4f793 Fetch VFP registers, not FPA. 2012-12-06 06:45:45 +00:00
apb
ee9a2498cf Adjust everything under src (but outside src/tools) to use
the TOOLDIR version of libnbcompat, associated include files,
and associated defs.mk file, instead of the version from the
.OBJDIR of src/tools/compat.  This should fix PR 47188.
2012-12-02 12:55:27 +00:00
joerg
66eae2a69d Merge r163231 from upstream to fix xulrunner build with Clang. 2012-11-08 18:13:53 +00:00
joerg
6677762418 Provide copy constructor and copy assignment operators for C++11.
Clang implements the C++11 semantics properly that require the default
to be implicitly deleted.
2012-11-08 11:24:00 +00:00
skrll
8f942710bb Re-run mknative for mips gdb 7.3.1 - not being used just yet. 2012-11-03 17:07:49 +00:00
skrll
7639cf466f Typo in previous 2012-11-03 15:07:40 +00:00
skrll
70142c72b9 Supply MIPS_ZERO_REGNUM and MIPS_UNUSED_REGNUM (as zero). Idea stolen from
mips-linux-tdep.c
2012-11-03 15:06:55 +00:00
skrll
2334c5671b Bring across target kvm support for mips from gdb6. 2012-11-03 14:59:44 +00:00
skrll
db35d67e76 Tidyup 2012-11-03 14:38:17 +00:00
drochner
d18545dea2 pull in upstream rev. 191413 to fix integer overflow in objalloc_alloc
(CVE-2012-3509)
2012-10-25 17:00:16 +00:00
msaitoh
237b58e244 Remove OLD manunal to install correct manual. 2012-10-12 18:41:59 +00:00
joerg
5af64d5574 PR 46978: ICE on spilling MMX registers
GCC/i386 has code to lower the required alignment for long long to 32bit
as the CPU doesn't need more. It is also using the same mode for setting
up the MMX registers and in turn, the stack slots reserved for spilling
require 32bit alignment. The actual vector types used keep the original
64bit alignment, so when the compiler wants to spill a MMX register, it
hits an assertion. Fix this by using the vector type as raw type for MMX
registers.
2012-10-06 14:10:46 +00:00
matt
04774ae728 This needs to have an #else clause 2012-09-26 05:57:45 +00:00
matt
40f28e9944 Fix _SOFT_FLOAT_ -> _SOFT_FLOAT 2012-09-26 05:38:29 +00:00
mrg
e8ae3e9a41 regen mknative files for GCC 4.5.4.
XXX: earm didn't build.
2012-09-18 19:45:46 +00:00
mrg
2c3eff6b3a regen mknative files for GCC 4.5.4. 2012-09-18 08:13:03 +00:00
mrg
67b559efa6 regen mknative files for GCC 4.5.4. 2012-09-18 07:44:34 +00:00
skrll
9378dd0cd5 Update for gcc 4.5.4 2012-09-18 07:05:15 +00:00
skrll
7ae732f19e Resolve conflicts. 2012-09-18 07:04:39 +00:00
skrll
a9d89c3b8a Import of gcc 4.5.4. The (possibly incomplete) list of fixed bugs is
50617 [4.5/4.6/4.7 Regression] ICE: RTL flag check: INSN_ANNULLED_BRANCH_P used with unexpected rtx code 'simplify_immed_subreg' in output_bb, at config/pa/pa.c:6631
  45383 [4.5 Regression] Implicit conversion to pointer does no longer automatically generate operator== and operator!=.
  45606 [4.5 Regression] match a method prototyped a typedef alias with the original type (using stdlib)
  47398 [4.5 Regression] tree check: accessed elt 10 of tree_vec with 9 elts in tsubst, at cp/pt.c:10500
  49951 [4.5/4.6/4.7 Regression] Debug stepping behavior regarding g++ Class destructor has changed for the worse starting at gcc 4.5.0
  43190 [4.4 Regression] Used pointer typedefs eliminated from debug info
  43866 [4.4 Regression] wrong code with -fbounds-check -funswitch-loops
  43897 [4.4 Regression] IA-64 asm clobbers are ignored
  44777 [4.4 Regression] ICE: SIGSEGV with -fprofile-use in gcc.c-torture/execute/comp-goto-2.c
  46985 [4.5 Regression] ICE: SIGSEGV in is_gimple_min_invariant (gimple.c:2742) with -fno-tree-ccp -fno-tree-dominator-opts -fno-tree-fre
  47780 [4.5 Regression] -fcompare-debug failure with -O -fgcse -fgcse-las -fstack-protector-all
  47858 [4.5/4.6/4.7 Regression] IPA-SRA decreases quality of debug info
  47903 [4.5 Regression] var-tracking.c: valgrind error
  48685 [4.5 Regression] ICE in gimplify_expr, at gimplify.c:7034
  52139 [4.5 Regression] ICE: in remove_insn, at emit-rtl.c:3960 with -O -fPIC -fno-tree-dominator-opts -fno-tree-fre
  48046 [4.5 Regression] Expected diagnostic "reference to 'type' is ambiguous" not given for function-local static declaration
  51406 [4.5/4.6/4.7 Regression][c++0x] Incorrect result of static_cast to rvalue reference to base class.
  43949 [4.4 Regression] bogus warning: array subscript is above array bounds
  45982 [4.4 Regression] PTA does not track integers
  48172 [4.5 Regression] incorrect vectorization of loop in GCC 4.5.* with -O3
  49115 [4.5 Regression] invalid return value optimization (?) when exception is thrown and caught
  49279 [4.5 Regression] Optimization incorrectly presuming constant variable inside loop in g++ 4.5 and 4.6 with -O2 and -O3 for x86_64 targets
  50189 [4.5 Regression] Wrong code error in -O2 [-fstrict-enums] compile, target independent
  48660 [4.5/4.6 Regression] ARM ICE in expand_expr_real_1
  23656 Cross-compilation with newlib fails in libiberty
  37985 [4.5/4.6/4.7/4.8 Regression] unsigned char shift lacks "statement with no effect" warning
  38292 [4.5/4.6/4.7/4.8 Regression] corrupted profile info with -O[23] -fprofile-use
  40778 [4.5 Regression] Mudflap instrumentation missing in cloned function.
  40992 [4.4 Regression] cunroll ignoring asm size
  48306 [4.4 Regression] presence of gcc subdir with . in PATH causes breakdown
  49651 [4.4 Regression] nested lambdas and -O3 produced incorrect integer variable increments
  52223 [4.5/4.6 Regression] libffi's man page install breaks with multilibs and overridden mandir
  53418 [4.5 Regression] ICE at gimplify.c:7773
  53138 [4.7 Regression] spaceship operator miscompiled
  50091 [4.5/4.6/4.7 Regression] -fstack-check generates wrong assembly
  50979 architecture mismatch: "mul32" not enabled for "smul" or "umul"
  51187 miscompilation of genrecog.c at -O2 for --target=avr
  52717 thunk referenced in discarded section when building samba with -flto
  48742 [4.5 Regression] Internal error in gimplify_expr
  49120 [4.5 Regression] bogus "value computed is not used" warning (variable-length array in compound statement)
  49161 [4.5 Regression] Fix VRP on switch stmts
  49619 [4.5 Regression] ICE in simplify_subreg, at simplify-rtx.c:5362
  49621 [4.5 regression] ICE in trunc_int_for_mode, at explow.c:57
  49644 [4.5 Regression] post-increment of promoted operand is incorrect.
  51767 [4.5 Regression] ICE with degenerated asm goto
  51768 [4.5 Regression] ICE with invalid asm goto
  52736 [4.5/4.6/4.7/4.8 Regression] miscompilation: store to aliased __m128d is 8 Bytes off
  49440 [4.6 regression] Invalid dynamic_cast for unnamed namespace
  50565 [4.5/4.6/4.7 Regression] initializer element is not computable at load time
  52294 [4.7 Regression] [ARM Thumb] generated asm code produces "branch out of range" error in gas with -Os -mcpu=cortex-a9
  41159 [LTO] ICE in insert_value_copy_on_edge, at tree-outof-ssa.c:225
  48822 [4.5 Regression] G++ gets stucks and never finishes compilation when enabling -O2/3 optimization options.
  50162 [4.5 Regression] Wrong vectorization
  49381 Unresolved symbols in libgcjgc.a when linking gctest
  45786 [4.5 Regression] Relational operators .eq. and == are not recognized as equivalent
  48708 Invalid V2DI vector set insn generated
  50464 Using -Ofast -march=bdver1 results in internal compiler error: in extract_insn, at recog.c:2109
  51821 [4.5/4.6/4.7 Regression] 64bit > 32bit conversion produces incorrect results with optimizations
  52698 -maddress-mode=long doesn't work
  53228 [4.6/4.7/4.8 Regression] target attributes in libcpp/lex.c cause illegal instructions to be used elsewhere
  42082 [C++0x] ICE on probably invalid with "canonical types differ for identical types"
  42652 vectorizer created unaligned vector insns
  42856 [4.4 Regression] FAIL: gcc.dg/torture/pr41555.c -O0 (test for excess errors)
  47733 psignal (int, const? char*) in libiberty/strsignal.h
  48743 -march=native mis-detects AMD K6-2+ / K6-3 as Athlon - compiled C fails with "illegal instruction"
  49038 [4.5/4.6/4.7 Regression] -ftree-vectorise introduces reads past end of array
  49448 arm-tab-linux-gnu-eabi enableds big endian when it should not
  49461 boehm-gc and gcj incompatible with pie
  50875 O3 and -mavx lead to internal compiler error: in find_reloads
  51161 [C++0x] Illegal static_cast to rvalue reference to ambiguous base class
  51393 Wrong parameter type for _mm256_insert_epi64 in avxintrin.h
  51444 [4.4 Regression]: Spurious "is used uninitialized" warning for structure with bitfields
  51835 ARM EABI violation when passing arguments to helper floating functions like __aeabi_d2iz
  52894 [4.5,4.6,4.7 Regression] Stage1 bootstrap fails with gcc-4.6.3: Infinite loop in pointer_set_insert
  53310 [4.5/4.6/4.7/4.8 Regression] EOSHIFT leaks memory
  53744 gcov version oscillates between 407* and 407p on branches
  52335 [4.4/4.5/4.6/4.7 Regression] I/O: -std=f95 rejects valid DELIM= in OPEN
  46192 [4.5/4.6/4.7 regression] wrong code for renaming of volatile packed array with address clause
  44581 [4.5/4.6/4.7 Regression] internal compiler error: in simplify_subreg
  49307 [4.5/4.6/4.7 Regression] ICE in spill_failure, at reload1.c:2113
  50163 [4.4/4.5/4.6/4.7 Regression] ICE: initialization expression
  50273 [4.5/4.6/4.7 Regression] -Walign-commons no longer effective
  52022 [4.5/4.6/4.7 Regression] Wrong-code with procedures passed as actual argument
  52452 [4.5/4.6/4.7/4.8 Regression] INTRINSIC cannot be applied to gfortran's ETIME
  25973 [4.5/4.6/4.7/4.8 Regression] Wrong warning: control reaches end of non-void function
  53521 [4.5/4.6/4.7/4.8 Regression] Memory leak with zero-sized array constructor
2012-09-18 06:09:45 +00:00
mrg
b2458df459 re-run mknative.
- i386 tested
- m68k gomp tls reverted by hand
- powerpc softfloat added (un-reverted) by hand
2012-09-18 05:31:32 +00:00
msaitoh
6fdd74c593 Fix gcc bugid 51408 for arm.
Fixes PR#46972.
2012-09-16 07:26:30 +00:00
joerg
af71fc1536 Fix GCC to correctly implement the i386 psABI on NetBSD.
This consists of two parts:
- for NetBSD/i386 and NetBSD/AMD64 with -m32, use a default stack
  alignment of 23bit as specified by the ABI
- ensure that double and long long variables on the stack are by default
  only aligned to 32bit, if there is nothing else in the function
  needing a larger stack alignment

The combination ensures that SSE variables on the stack trigger the
realignment logic, but just using double or long long doesn't.
2012-09-14 13:00:01 +00:00
martin
6d25cb1840 Make can_trust_pointer_alignment() always return false on STRICT_ALIGNMENT
archs - gcc 4.5 is not able to properly track alignment and backporting
the fix from 4.6/4.7 is not feasible (according to upstream).
See http://gcc.gnu.org/bugzilla/show_bug.cgi?id=46483 for details.
Fixes PR toolchain/46865.
2012-09-02 20:58:44 +00:00
msaitoh
568a3a3a5a Don't add unwind.h stuff into BUILDSYMLINKS when MKGCC=="no".
Fixes "Wrong number of words (1) in .for substitution list with 2 vars" problem
while mknative-ing. Approved by mrg.
2012-08-29 03:12:08 +00:00
matt
7d57bc60df Make this to produce working shared libraries again.
Resultant distribution was booted into single user using shared libraries.
2012-08-27 16:50:14 +00:00
matt
7c4c75c298 Add support for setting LIB_PATH for MKCOMPAT support. 2012-08-13 02:52:34 +00:00
mrg
99a54d3479 pay attention to -pie: link crt{begin,end}S.o.
this fixes -fpie on sparc and sparc64, and probably others.
2012-08-12 00:01:50 +00:00
joerg
c14f2d4ef8 Deal with optional HAVE_GCC. 2012-08-10 16:05:26 +00:00
matt
a4ae934e29 Remove code that should be have excised a long time ago. 2012-08-07 01:09:13 +00:00
matt
cb8c048ec5 on earm, don't include EH code. 2012-08-06 02:34:28 +00:00
matt
e19c6b7318 Add LIB2_EHASM to SRCS 2012-08-06 01:38:29 +00:00
matt
267745d7dd More regened configury (mostly exception related). 2012-08-06 00:49:52 +00:00
matt
c73e5095cc a few more fixes (make unwinding correct for EABI)
improve link spec to with fix-v4bx and emulations
Add bpabi-netbsd.c to resolve problem with bpabi.c conflicting with bpabi.S
2012-08-06 00:24:13 +00:00
matt
5598cdb53e Regen again. 2012-08-06 00:21:37 +00:00
matt
93f7a012df Deal with LIB2_EHASM 2012-08-06 00:21:09 +00:00
matt
638a65b2c0 deal with LIB2_EH has ASM (.S) files. 2012-08-06 00:19:03 +00:00
matt
b626930d34 Add a few missing for earm's gcc configury 2012-08-05 17:21:47 +00:00
matt
015ce606f7 Add gdb configury for earm 2012-08-05 17:09:16 +00:00
matt
714ce8eeef gcc4.5.3 configury for earm 2012-08-05 17:03:31 +00:00
matt
cd8b5f8c57 Allow arm*-netbsd*-eabi* to be recognized. 2012-08-05 16:51:46 +00:00
matt
88a901ba99 binutils mknative run for earm 2012-08-05 16:34:05 +00:00
matt
602e0146d8 Add arm{,eb}--netbsdelf-eabi support. (still evolving) 2012-08-05 04:10:18 +00:00
matt
ad73c53594 Add arm{,eb}--netbsdelf-eabi support. 2012-08-05 04:03:03 +00:00
joerg
e7a9d9d117 Remove a bunch of broken inline qualifiers that break the -O0 build. 2012-07-20 21:18:00 +00:00
christos
edd104c76c PR/46704: Antti Kantee: Recognize tilera in config.guess 2012-07-19 19:34:26 +00:00
matt
b7c801cac8 Two fixes. Better PLT pruning (don't emit PLTs for local functions).
If emitting a reloc against a readonly section in a shared image,
cause TEXTREL to be set.
2012-07-17 21:37:21 +00:00
matt
ec769e4972 Warn about using a symbol as a displacement in PIC mode. 2012-07-17 20:29:44 +00:00
abs
86aebb49c7 Switch -current vax back to gcc 4.1 to match netbsd-6 - until someone has
time to look at the gcc 4.5 codegen issues we should at least have a usable
-current for vax.
2012-06-22 20:32:34 +00:00
martin
4d5a9c43e0 Apply upstream revision 175141: setjmp vs. unchanged register values;
should fix PR toolchain/45837.
2012-06-17 13:43:30 +00:00
christos
15053c8b40 add specs to automagically add the mudflap libraries when -fmudflap{,th} 2012-04-27 00:57:44 +00:00
christos
cbd0c35a2d remove code that assumed that lwpid shares pid space and can be used interchangeably. 2012-04-24 19:14:06 +00:00
christos
7006e67fd8 Bring in fix from:
http://gcc.gnu.org/bugzilla/show_bug.cgi?format=multiple&id=43804
Allows libmudflap to compile on m68k:

/usr/src/external/gpl3/gcc/dist/libmudflap/mf-hooks1.c: In function
'__mf_wrap_alloca_indirect':
/usr/src/external/gpl3/gcc/dist/libmudflap/mf-hooks1.c:492:1: error:
insn does not satisfy its constraints:
(insn 360 142 68 13
/usr/src/external/gpl3/gcc/dist/libmudflap/mf-impl.h:257 (set (reg/f:SI
6 %d6 [159])
        (const:SI (unspec:SI [
                    (symbol_ref:SI ("__mf_state_1") [flags 0x50]
<var_decl 0x7f7ff7304d20 __mf_state_1>)
                     (const_int 1 [0x1])
                 ] 6))) 36 {*movsi_m68k}
(nil))/usr/src/external/gpl3/gcc/dist/libmudflap/mf-hooks1.c:492:1:
internal compiler error: in reload_cse_simplify_operands, at postreload.c:396
2012-04-22 15:15:46 +00:00
christos
3fd38f84eb If we are asked to step on ptid(-1,0,0), then step on our inferior_thread
instead, which is the main thread instead of the currently executing thread
which is not what we want, since we've been running and nother thread might
have just started.
2012-04-21 00:16:35 +00:00
christos
49a655adee Make declarations consistent, and change unsigned int to unsigned long so
that this works on LP64 machines. Why is the __mf_uintptr_t needed anyway?
2012-04-19 15:52:39 +00:00
christos
9175dee1fe bad name 2012-04-18 22:42:21 +00:00
christos
6e275ac292 add the mudflap include and libraries 2012-04-18 19:22:03 +00:00
christos
6b798f149f move include to the gcc-4.5 subdir. 2012-04-18 19:21:25 +00:00
christos
f89a1d6f2b NetBSD fixes:
1. thread_self() returns a pointer, not an unsigned integer
2. Add NetBSD to Apple and FreeBSD defines
3. Add _NETBSD_SOURCE where needed
4. Add an extra define BEGIN_PROTECTV for void functions to avoid return
   free(); where free is void.
5. Avoid weak symbol hacks to determine if we are threaded or not. We
   have a threaded copy of the library, why bother?
6. change __attribute -> __attribute__ since the former is not covered by
   our cdefs.h
2012-04-18 02:55:05 +00:00
christos
d0800ba09f add preliminary build glue for mudflap; only the shared libraries work,
the static ones will need us to add __real_foo aliases for a bunch of
functions in libc.
2012-04-18 02:52:07 +00:00
christos
16918ffb5d - In the thread activation code, mutate the main thread (lid=0) to lid=1 like
the kernel does.
- Remove - 1 hack
- Remove more ifdef notdef code
2012-04-11 21:41:59 +00:00
christos
4ae881aba3 On NetBSD the data part of the PT_STEP request is the lid to send the signal,
not the signal to send! Make it so.
2012-04-11 21:39:01 +00:00
christos
defdde4f72 remove more unused SA userland thread stuff. 2012-04-11 20:21:35 +00:00
wiz
be5cf4dc86 clang complains:
C++ default arguments are illegal in the function defininion.
christos@ ok
2012-04-09 00:24:57 +00:00
he
692082ea92 Disable HAVE_TLS for now for gcc's libgomp, since it otherwise
causes gcc indigestion (internal compiler error) for all m68k ports.
mrg@ says this will do for now, and committing to this generated-
by-mknative file is ok.
2012-04-06 20:10:28 +00:00
mrg
829e755fe2 rerun mknative-gcc:
- turn off <fenv.h> on platforms that don't have it
2012-04-05 21:09:20 +00:00
christos
49758559c7 - remove unused thread (non-lwp) code.
- make the get method return the value, and only add 1 in the put method.
2012-04-04 13:33:19 +00:00
joerg
b757af438b Disable new -Wstring-plus-int warning where needed for now.
Adjust various places that add GCC-only options to check for the active
compiler first.
2012-04-04 10:59:44 +00:00
christos
92a9368199 only +1 for the 0'th thread (if we did not find any other) 2012-03-22 16:06:01 +00:00
christos
2f9576aacc complete the mapping of the lwp -> (lwp - 1), by adding 1 where appropriate. 2012-03-22 15:26:32 +00:00
christos
24da109f75 Use tid - 1 for the thread id, so that thread 1 matches the main thread
before the threaded code gets loaded. fixes spurious breakpoints. Is
there a better way?
2012-03-21 23:20:58 +00:00
christos
9b33eb8aa1 Undo previous, it was wrong:
The problem has to do with the threaded initialization.
After we take the first breakpoint and we enter single step mode,
we set trap_expected = 1 in the thread_info structure for main <pid,0,0>.
After the threads initialize, the main thread becomes <pid,1,0>, and so
we get a new thread_info struct with trap_expected = 0, and so we break.
2012-03-21 21:25:38 +00:00
christos
436a58b1ab Disable OS supplied single step functionality, because the code here is
wrong.
2012-03-21 18:01:34 +00:00
wiz
e93c7961c5 Sync usage with man page. 2012-03-19 09:14:15 +00:00
wiz
34e2e47694 New sentence, new line.
Sort descriptions.
Use simpler markup.
Bump date for previous.
2012-03-19 09:13:33 +00:00
bsh
f4eb9f64cb adjust the size of db_symtab space automatically.
proposed on tech-toolchain@, and got no objections.
2012-03-19 05:38:26 +00:00
joerg
4acff4c01b Implement sem_timedwait. 2012-03-08 21:59:24 +00:00
matt
6be8dcf23e Fix merge botch dealing with linker assignments. 2012-03-04 17:09:32 +00:00
matt
82cfc8036f Fix support for .protected symbols. 2012-03-02 16:37:16 +00:00
joerg
de785a6e75 gdb likes to mix different enum types in switches, so disable the check
for clang.
2012-02-28 22:07:54 +00:00
joerg
14ac342e56 Don't use clang here. 2012-02-28 20:26:07 +00:00
christos
268a453af7 PR/46068: Fix symbol loading on i386 kernels. On i386 lma != vma and gdb7
depends on them being != to detect overlays and avoid loading them. I've
disabled the test for now.
2012-02-24 22:41:12 +00:00
nonaka
6e76caabe4 fix build failure on mips64. 2012-02-23 11:05:02 +00:00
mrg
97a48de011 avoid bfd.info rebuilds and r/o source lossage. 2012-02-18 06:17:39 +00:00
nakayama
b3ed3f9f74 The default configuration for TLS support is supposed to use Sun
as, but we use GNU as.  So in this case it generates wrong
relocations in non-PIC mode.

This change fixes lib/libc/tls/t_tls_dynamic test failure on 32-bit
sparc as described in PR toolchain/45985.

Approved by releng.
2012-02-14 11:25:05 +00:00
matt
3ffd030673 Fix problem leading to triggering a BFD assert: when allocating space in the
got, do not allocate slots for symbols without default visibility.
2012-02-10 01:47:37 +00:00
skrll
03fa5d214f Make mips gdb7 compile.
XXX not sure I got this right.
2012-02-09 15:14:19 +00:00
skrll
c49a22327e Re-re-run gdb7 mknative for mips. mips not using gdb7 yet.
OK martin@
2012-02-09 15:13:30 +00:00
skrll
6b25048fe3 Re-re-run mknative for vax on gdb7.
vax isn't currently using gdb7 so this doesn't hurt anyone and I'm going
to ride my previous OK from releng :)
2012-02-09 15:05:00 +00:00
skrll
0cb5c6eccd Re-run mknative.
OK releng@ ack 3 nak 0
2012-02-06 10:55:32 +00:00
skrll
69352bd310 Add nbsd-pthread.o.
OK releng@ 3 ack 0 nak.
2012-02-06 10:46:34 +00:00
matt
5a1411907d For VAX & GCC, turn on -Wno-overflow to supress a GCC error. 2012-02-05 17:47:30 +00:00
matt
2c2478331f Gcc emit overflows warnings on VAX when you try to use HUGE_VAL. Make these
warning supressable if -Wno-overflow is given.
2012-02-05 17:43:47 +00:00
matt
c1538b0e12 Deal with vax defining [an empty] struct fpreg;
Add supply_gregset and fill_gregset for nbsd-thread.c to vaxbsd-nat.c
2012-02-05 17:40:48 +00:00
matt
512e444044 Use REG_P, CONST_INT_P, and gcc_unreachable().
Bring forward movememsi from gcc4.1
2012-02-05 17:38:21 +00:00
matt
a7e9fdf4f5 Constraint 'T' needs to be a CONSTANT_P so add a match_test for that. 2012-02-05 17:37:19 +00:00
skrll
80a78e2456 Fix build of gdb7 for mips. It's not used at present. 2012-02-05 13:26:01 +00:00
drochner
28af654232 tell the compiler that the i387 runs in double-rounding mode, so it
doesn't need to issue memory store-read sequences to kill excess
precision. makes code smaller and faster, depending on optimization
flags
(as tests on Linux have shown, the compiler doesn't even succeed in
avoiding excess precision)
2012-02-02 13:07:33 +00:00
dholland
59b296daa7 Change the syscall API for quotas over to the new non-proplib one.
- struct vfs_quotactl_args -> struct quotactl_args
   - add sys/stdint.h to sys/quotactl.h for clean userland build
   - install sys/quotactl.h in /usr/include
   - update set lists for same
   - add new marshalling code in libquota
   - add new unmarshalling code in vfs_syscalls.c
   - discard proplib interpreter code in vfs_quotactl.c
   - add dispatching code for the 14 quotactl ops in vfs_quotactl.c
   - mark the proplib quotactl syscall obsolete
   - add a new syscall number for the new quotactl syscall
   - change the name of the syscall to __quotactl()
   - remove the decl of the old quotactl from quota/quotaprop.h
   - add a decl of the new quotactl to sys/quotactl.h
   - update the libc build
   - update ktruss
   - remove proplib marshalling code from libquota
   - update copy of syscall table in gdb ppc sources
   - hack rumphijack to accomodate new quotactl name (as I recall,
     pooka wanted such a name change to simplify something, but I
     don't really see what/how)

This change appears to require a kernel version bump for rumpish
reasons.
2012-02-01 05:34:38 +00:00
joerg
48d38253ab Disable -Wconversion for clang. 2012-01-28 14:24:53 +00:00
joerg
dec45735b2 Merge r171807 from upstream:
exception_ptr.h needs the forward declaration because it's
included from <typeinfo> before <typeinfo> defines std::type_info.
2012-01-28 14:21:52 +00:00
uwe
6b9feef6d1 Pull in revision 1.4 from src/gnu/dist/gcc4/gcc/config/vax/elf.h:
Emit DWARF relocation in its expected form

PR toolchain/43314
2012-01-28 11:24:05 +00:00
christos
669aa7297a make powerpc compile. 2012-01-25 19:24:21 +00:00
christos
da2b6379c3 hack to make sh3 build. 2012-01-25 17:01:02 +00:00
christos
7c79471a43 Deal with sh3 having no FPREGS and having 32 bit pointers and 64 bit CORE_ADDR.
Ugly.
2012-01-25 16:48:44 +00:00
christos
bf1e6562d5 fix this properly. 2012-01-25 16:25:28 +00:00
christos
3fb02d96a3 make thi 2012-01-25 16:21:22 +00:00
christos
525fde84b9 make gdb link again 2012-01-25 16:08:37 +00:00
christos
6dc91634bc remove error(1) junk. 2012-01-25 03:26:39 +00:00
christos
3010244ff3 Fix i386 2012-01-25 03:25:02 +00:00
martin
8d947a05b5 Use void* instead of pr{f,}pregset_t for now to make it compile. 2012-01-23 21:51:46 +00:00
christos
7a2aab3e0e add {fill,supply}_{g,fp}regset(), completely untested. 2012-01-23 21:28:40 +00:00
christos
b820deae47 add supply_{g,fp}regset() 2012-01-23 21:24:43 +00:00
skrll
5968222aaf Provide {supply,fill}_{g,fp}regset 2012-01-23 06:17:58 +00:00
skrll
4a46d474d5 Provide {supply,fill}_{g,fp}regset 2012-01-22 22:04:48 +00:00
skrll
564cf36b7d More cheating wrt mknative 2012-01-22 20:38:56 +00:00