Add missing include <stdlib.h>

(martin)

Fix quota2 list corruption issue when defaultquotas are 0 (deny any file
and block allocation).

When quota2_check() is called with an uid not yet in the list,
getinoquota2() will call quota2_q2ealloc() to allocate a new entry for this
uid. quota2_q2ealloc() will remove an entry from the free list and
put it at the head of the corresponding hash list, and flush the block
containing the header if it's not the one also containing the allocated entry.
quota2_q2ealloc() then return the alocated entry and corresponding block
to caller (getinoquota2() here), which returns it to quota2_check().
quota2_check() then checks if the allocation can succeed, and returns and
error if not and calls brelse() on the buffer (because from his POW no
change was made to the entry), effectively discarding changes
to the entry that may have been made by quota2_q2ealloc().
Fix by always bwrite()ing the entry in quota2_q2ealloc(), and re-reading
the entry in caller.

(bouyer)

deal properly with empty lines in spec file

(christos)

Add some more debugging messages.

(matt)

Add regression test for cdbr(3) and cdbw(3).

(joerg)

make the test more precise.

(christos)

Don't refuse the open databases without entries or keys, just protect
the divisions. cdbr_find and cdbr_get already have the appropiate
checks.

(joerg)

Don't initialize PCIe inbound windows.  This avoids the 256MB limitation
on DMAs.

(matt)

Add vendor name.

(matt)

Add DSB

(matt)

Don't bother dealing with "extra" ticks, just count them.

(matt)

Print out u-boot args

(matt)

now sense -> no sense

(joerg)

add and document AF_LOCAL (and the rest that were not)

(christos)

fix non-numeric address and port printing.

(christos)

Fix year.

(joerg)

npf.conf(5): improve and explain grammar definition.

(rmind)

If we get a fault we shouldn't have, set pmap_needs_pte_sync and retry.

(matt)

Fix in comment.

(msaitoh)

Remove expected failures that no longer fail (probably due a Qemu update).

(jruoho)

This needs to have an #else clause

(matt)

Fix _SOFT_FLOAT_ -> _SOFT_FLOAT

(matt)

Simplify the BDZ compression function, making it smaller at the same
time. Fixes a bug where non-minimal hash functions could be created.
Add regression tests for BDZ, including the map output functionality.

(joerg)

Check tmpfs_rmdired_p after tmpfs_vnode_get when walking up the tree.

tmpfs_vnode_get drops all locks except possibly the reclaiming bit
lock to keep the tmpfs node from being reclaimed while we're still
interested in it.  Consequently, it does not keep the directory's
existence invariant, so we must check that after tmpfs_vnode_get.

Fixes PR kern/46990.  Tested by Wolfgang Stukenbrock.

(riastradh)

Sort -h option properly (not between -I and -i)

XXX Should the date be updated?

(pgoyette)

No need to do "obj includes" twice.

(skrll)

More tweaks. I didn't manage to complete a mknative from scratch run, but
this is a step in the right direction.

(skrll)

Add Lava Computers SSERIAL-PCI single port serial PCI card.

(gson)

regen

(gson)

Add Lava Computers SSERIAL-PCI single serial port adapter.

(gson)

Back out 1.12 and include a comment as to why.

(matt)

Enable support for synaptics touchpads when running Xen as domain 0; helps
usability on laptops. Fixes PR port-xen/44055.

ok bouyer@ riz@

(khorben)

Fix setsockopt(2) error on 64bit environment (amd64).

Reported by PR lib/46693 by me and OK'ed by dholland@.

(taca)

Add missing "\n" in log(9)

(msaitoh)

increase powerpc NKMEMPAGES_MAX_DEFAULT to 256MB.  remove the macppc
overrides that are now the same as the powerpc default.

(mrg)

Disable a lot of debug output which would show up if you change from the
xserver to another console and back

(veego)

update for xf86-video-ati 6.14.6

(veego)

merge xf86-video-ati 6.14.6

(veego)

initial import of xf86-video-ati-6.14.6.

NetBSD note: The libdrm requirement seems to be KMS related which we do
            not have.

* 6.15.6
  This version requires the latest libdrm 2.4.36 release, and fixes a few
  other bugs seen since 6.14.5.
* 6.14.5
  - add solid picture accel
  - tiling fixes
  - new pci ids
  - 6xx-9xx Xv improvements
  - support for upcoming xserver API changes
  - bug fixes

Status:

Vendor Tag: xorg
Release Tags: xf86-video-ati-6-14-6

(veego)

Revert two unintentional changes from the PPC tests

(joerg)

Prevent sysinst from setting an fqdn in rc.conf when the user entered no domain
(i.e., sets only the hostname).  Fix for PR install/46946.

(jdf)

Update LLVM/Clang snapshot to r164464. This adopts the GCC options for
the SSP parameters and a not-yet-default rewrite of SROA.

(joerg)

Map 1M beyond _end to make sure we bootstrap.

(skrll)

Don't use a usbd_status as an int, split error into two variables.

(joerg)

Wrap sbuserr_handler and sbus_error with:
  #if (defined(SUN4M) && !defined(MSIIEP)) || defined(SUN4D)
to give them the same scope as the definitions in ../sparc/intr.c.
Allows SUN4C-only kernels to compile.
OK mrg

(jdc)

correct some comments on #endif to match their #if.

(mrg)

add more sd and pci devices.
remove duplicate ch0.

(chs)

remove a debug printf.

(chs)

add entries for AOE and FCOE.

(chs)

don't try to handle sensors if there aren't any.

(chs)

set chan_bustype correctly.

(chs)

reformat product array to match openbsd.

(chs)

use 64-bit DMA where possible.

(chs)

fix a debug printf.

(chs)

match some more devices.

(chs)

add an entry for subclass HD audio.

(chs)

regen

(chs)

add a bunch of devices.

(chs)

add a bunch of devices.  from openbsd.

(chs)

regen

(chs)

add a bunch of devices.  from openbsd.

(chs)

add vmt entry to GENERIC.
standardize commented pfsync and npf entries.

(chs)

add some more devices and options.

(chs)

sync ldscripts; add cacheline_aligned and read_mostly handling
to the non-default ones.

(chs)

locate PCI buses and determine their bus numbers using the info
previously extracted from ACPICA rather than trying to figure it out again.
allow PCI buses that don't have a _PRT method.

(chs)

re-enable the code to disable link devices at startup, ie. revert rev 1.3.
this fixes PCI interrupts on some systems (eg. HP XW9400) and we suspect that
the problems which led to the original change were caused by buggy early
implementations of ACPI, which are now ignored by date.

(chs)

LINUX_RLIM_INFINITY doesn't fit into the value range for linux32, so
introduce a variant with correct value.

(joerg)

Disable L2 cache for now.  Add phys for wm

(matt)

Add FPU_VFP option

(matt)

Only use CPACR register for ARM11 and CORTEX cores.
Add VFP ids for other CORTEX CPUs.

(matt)

Fix PR kern/46828 (6.0_BETA2 and 6.0_RC1 won't start on DL320/G5p):
In ehci_get_ownership(), don't explicitly clear EHCI_LEG_HC_BIOS_OWNED
semaphore bit in the driver before asking BIOS to give up ownership.
The EHCI spec implies that the semaphore should not be changed by
the other agent and actually the previous one (introduced in rev 1.53
after 5.x) caused hangup during probe on at least two HP machines
as mentioned in the PR.  Analyzed and patch provided by Ryo ONODERA.

Should be pulled up to netbsd-6 (fatal hangup during boot).

(tsutsui)

Make sure that the "to fix, run: ..." instructions actually work cut-and-paste
By default postinstall has mode 644 so /bin/sh or similar needs to be prepended

(ast)

Add busaddr to paddr routine and use it.
cleanup the PREREAD sync case.

(matt)

Add interrupt/iwin/owin / netbsd_configure code.

(matt)

PCIE each have 6 interrupts

(matt)

Add a few more PCIE registers

(matt)

Before testing for VFP, make sure CP10 is enabled.  (And CP11 for Neon too).

(matt)

Don't use an asm in pmap_activate to update the TTBR, use cpu_setttb instead
but add a second argument to it to indicate whether the TLB/caches need to be
flushed.  Default cortex to pmap_needs_fixup = 1.  But check the MMFR3 field
to see if the fixed can be skipped.
Use a cf_flag bit 0 to indicate whether the A9 L2 cache should disable (bit 0 = 1)
or enabeld (bit = 0).

With these changes, the A9 MMU can use traverse caches to do MMU tablewalks
Also, make sure all memory has the shareable bit for the A9.

(matt)

Add a 'mach fault' command to print DFAR/DFSR/IFAR/IFSR/TTBR

(matt)

Don't use NODEV when comparing against a major number as this is an
impossible type mismatch.

(joerg)

For the rumpsp protocol, don't assume that the bit representation of
errnos match on the client and server platforms (the syscall subprotocol
errnos are handled by the server compat code).

(pooka)

Switch to the generic bounce buffer support.

(matt)

Switch to the generic bounce buffer support.

(matt)

Add APIPA

(ginsbach)

adapt for _UC_TLSBASE.

Approved by manu@ and msaitoh@

(ryo)

Fix npf module paths

(martin)

Mention that gcc-4.5.4 was imported and that 4.7.2 is out.

(wiz)

Fix an inverted test

(agc)

support anti-aliased fonts, glyph caching etc.

(macallan)

Fix device timeout problem.
- Change the synching order of descriptors. First, sync descriptors except
  first and then sync the first descriptor.
- To recover from an race condition, reduce the if_timer from 5 to 1 and
  when timeout occur write MVGBE_TQC_ENQ bit again.

(msaitoh)

Fix whitespace (mostly removing trailing).

This commit changes only whitespace (trailing, tabs vs spaces,
removing spurious newlines).  From Bev Schwartz of BBN.

(gdt)

Correct name of the less version.
Patch provided by Snader_LB (Freenode).

(jdf)

add back old options for compatibility, but complain if specified.

(christos)

sc_ahci_cap should be uint32_t

(matt)

sort stubs, remove autonamespacing and add some signal-related ones
I missed yesterday

(pooka)

regen

(pooka)

alias rump_sysent to sysent, since the linux compat code wants to
access it (it calls ptrace, so 0 practical impact here, though).

(pooka)

fix EXTERNAL_TOOLCHAIN build

(pooka)

strip trailing whitespace - noted by Snader_LB on IRC

(abs)

regen

(abs)

Adjust postinstall recommendation syntax. based on comment from Snader_LB on IRC

(abs)

Fix string_to_flags prototype. From Brooks Davis in PR 46986.
Bump date.

(wiz)

strip trailing whitespace

(abs)

Fix inverted logic description for MKSTRIPIDENT.
Noted by Snader_LB on freenode IRC

(abs)

gen (without re)

(pooka)

Add the first attempt at rump kernel support for Linux clients.  This has
been lightly tested with unmodified networking applications with both
the client and server on a 64bit le host.  Unlike the standard Linux
compat libs where args and syscalls are swizzled around, this compat
lib only massages the arg data types due to the assumption that syscall
numbers come from librumpclient (via librumphijack) and therefore match
the native NetBSD numbers.

(pooka)

Note mfi(4) ioctl pass-through

(bouyer)

regen for ppoll (and, apparently, SYCALL_ARG_PTR)

(pooka)

Add a pass-through ioctl for mfi(4), allowing userland to send raw commands
to the controller. This is compatible with the linux and FreeBSD
implementations.
Add the needed conversion for mfi ioctls in COMPAT_LINUX
Allocate a character major number, and create /dev/mfi0 by default
on amd64 and i386.
This allows (along with a hand-created /emul/linux/proc/devices file)
to run the MegaCLI linux binary provided by LSI.

(bouyer)

emulate ppoll which is essentially our pollts

(pooka)

Use the PROM mapping for the clock, if it exists.
Allows the clock on the Tadpole SPARCle to attach.
Idea from r1.43 of OpenBSD sys/arch/sparc64/sparc64/clock.c

(jdc)

Does not make sense to mount this as NFS, so it is not a bug.
We can now mount multiple instances, but all of them show all the ptys.

(christos)

* Add scanw family function calls as input functions

(blymn)

* Fix mvscanw return
* Fix the *vline family of calls, one argument is chtype not int

(blymn)

Define ISCSI_HTONLL6 and ISCSI_NTOHLL6 (6 byte network byte order accessor
macros) dependend on host endianess.
Spotted by mhitch, unfortunately not enough to fix iscsi-target problems
on sparc64.

(martin)

Use .inst instead of wfe/sev to shut up gas.

(matt)

make Netwalker kernel compile again.
from Kenichi Hashimoto.

(bsh)

Match the Altera ebus bridge, as found on the Tadpole SPARCle.

(jdc)

less-451 out.

(wiz)

some older powerbook keyboards use the same scancode for the power button as
later ones send on Fn-Command - now we look for that 'special' scancode only
on keyboards that actually need it

(macallan)

let us get mounted multiple times.

(christos)

remove -c and chroot option; they are always on now

(christos)

Always do the chroot filename mapping; it is pointless not to do it.

(christos)

regen mknative files for GCC 4.5.4.

XXX: earm didn't build.

(mrg)

Take better care of closing file descriptors in the agent child and dealing
with dup2 and std{in,out,err}.

(christos)

Fix MKDEBUG set lists

(skrll)

Add ./usr/libdata/debug/usr/lib/npf for rmind

(skrll)

Enable bounce buffers

(matt)

Enable bounce buffers

(matt)

Remove bounce buffer support since there is now generic bounce buffer support

(matt)

npf extension modules for evbppc abi variants

(martin)

npftest.conf is not dependend on pic

(martin)

Try to make this test gracefully fail when npftest is not available

(martin)

regen mknative files for GCC 4.5.4.

(mrg)

regen mknative files for GCC 4.5.4.

(mrg)

regen mknative files for GCC 4.5.4.

(mrg)

Update for gcc 4.5.4

(skrll)

Resolve conflicts.

(skrll)

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

Status:

Vendor Tag: FSF
Release Tags: gcc-4-5-4

(skrll)

Add bounce buffer support for ARM bus_dma(9).  Add macros to help initialize
bus_dma_tag structures.

(matt)

re-run mknative.

- i386 tested
- m68k gomp tls reverted by hand
- powerpc softfloat added (un-reverted) by hand

(mrg)

add _ARM32_NEED_BUS_DMA_BOUNCE to opt_arm_bus_space.h (It's not really a
bus_space option but it's close enough).

(matt)

Regen.

(matt)

Fix tpyo.

(matt)