Name global variable for routing socket rtsock like in ndp(8).
OK florian@

Let ndp(8) use the process's current routing table by default.
from Pierre Emeriaud;  OK jca@ claudio@
Sync code and man page with arp(8).  OK florian@

The tlb flushes in pmap_set_{l1,l2,l3} use ranges that don't fully make sense.
But those tlb flushes shouldn't be necessary anyway, so simply remove them.
Simplify the tlb flushing code now that we no longer flush ranges, and
revive the branch that doesn't flush a specific ASID for the kernel pmap
since its mappings are global.

ok patrick@, visa@

Handle R_SPARC_WPLT30 relocations against a local symbol.  Fixes building the
audio/openal port with clang.

ok guenther@

regen

update to 4.1.16rc1
tests & OK sthen

(if there are more changes coming for 4.1.16 release we will just
commit them on top)

Fix format string in ACPI_MEMDEBUG block

From Anton Lindqvist (anton.lindqvist(at)gmail.com)

Sync bus_dmamap_load_raw() with amd64 for better constraint checking.
Needed by xhci(4).

No GMX on CN73xx.

mark newish phony targets as phony.
okay tb@

Remove unused define satoin6().

Pass down the address family through the pr_input calls.  This
allows to simplify code used for both IPv4 and IPv6.
OK mikeb@ deraadt@

adjust .Lk tests after groff and mandoc .Lk improvements

once cvs's flow-control mechanism has kicked in, stop reading from
its local reader until memory usage goes back down below its
watermark.

during a checkout of a tree with big files (like www) from a fast
reader (disk) and a slow writer (net), the amount of data being
buffered can back up enough that cvs tries to allocate too many
buffers and hits its resource limit, causing death.

cvs's flow-control mechanism properly detects this early on, but the
message sent to the reader process to stop sending data takes too
long to process.

take more aggressive action and just stop reading from the reader
until the writer has ejected enough data that it can start re-using
its already-allocated buffers instead of allocating new ones.

ok deraadt

Show long .Lk URIs in like an indented display, similar to groff.
Suggested by bentley@.

Add test for IP payload compression.  It is sending small and big
ping packets as only the latter get actually compressed.

Do not make the colon after the .Lk link text italic.
I just pushed the same change to GNU troff.

Do not make the colon after the .Lk link text italic.
I just pushed the same change to GNU troff.

Add tests with the ipsec.conf SA bundle keyword.

Up to now ipsecctl(8) grouped SAs with identical src and dst to the
flow which the first SA matched by the flow type.  This behaviour
was mostly undocumented and unexpected.  Make SA bundles explicit
in ipsec.conf(5).  Only group SAs that have the same src and dst
and also the same bundle identifier.
OK hshoexer@

Use freezero(3) when cleaning up session tickets - not only does it require
less code, but there is also a potential performance gain since they can be
larger allocations.

Use freezero(3) to clean up the X25519 keys - simpler, cleaner code.

Use freezero(3) in the CBB clean up path, since this could hold sensitive
information (such as master keys).

Switch i2d_SSL_SESSION() back to freezero(3) now that the size constraints
have been relaxed.

Clean up server key exchange EC point handling. Encode the point directly
into the CBB memory, rather than mallocing and memcpying, which also makes
makes the code more consistent with the client. Add a missing check for the
first EC_POINT_point2oct() call.

ok beck@

Avoid some false positives with cppcheck.  No binary change.
OK jsg@

whitespace

Define __dead and __pure even if __STRICT_ANSI__ for compilers that
support GCC's __attribute__ syntax.  Fixes several warnings when compiling
code with clang with -std=c++11 or some other strict ISO standard.

ok millert@, guenther@

correct path; from Klemens Nanni

SVM: calculate max ASID value and save for later use. This will be used in
an upcoming diff to handle ASID/VPID reuse/rollover.

Update a man page example to reflect recent changes.

Spotted by Ilya Kaliman, thanks.

A little bit more trivial cleanup.

Xr sigprocmask(2) not the obsolete sigsetmask(3)

Use the non-interrupt-safe pool allocator for the vp pool to avoid runninng
out of kva in the kmem_map.  Avoids a hang when spawning a lot of processes.

Use recallocarray in getdelim/getline to clear memory on buffer resizes,
inspired by a similar change to fgetln.

ok deraadt millert

allow clearing less than allocated and document freezero(3) better

moving some code into a switch meant that break no longer stopped the loop.
try harder with a goto. diagnosis and original fix by tb.

Remove a bunch of obsolete, unused and irrelevant DHCP client types, fields,
and enums.

multi-statement CHECK_RANGE() macro isn't safe for all placements, and
needs to use "do {} while 0" idiom; all callers need repair also.
Discovered by jsg

fix wrongly indented lines

Add a NAT-T keepalive timer in case we are behind a NAT gateway.

See RFC 5996, section 2.23, NAT Traversal:
  In the case of a mismatching NAT_DETECTION_DESTINATION_IP hash, it
  means that the system receiving the NAT_DETECTION_DESTINATION_IP
  payload is behind a NAT and that system SHOULD start sending
  keepalive packets as defined in [UDPENCAPS].

With markus@, ok reyk@

regen

Delete the getlogin59 syscall, which was last used one year, two releases,
and four libc major versions ago

ok sthen@ jsing@ deraadt@ jca@

Provide mips64 with kernel-facing TCB_{GET,SET} macros that store it
in struct mdproc.  With that, all archs have those and the __HAVE_MD_TCB
macro can be unifdef'ed as always defined.

ok kettenis@ visa@ jsing@

Inspired by recent dhcrelay changes, bring in stricter CFLAGS!

One 'foo' per function is enough. Rename one to eliminate shadowing.

Add missing function prototypes. Mark kw_cmp() as static like all
its friends.

The kernel has to slightly different version of SipHash_Final but with
the same bug as just fixed in userland:

----------
SipHash_Final() was assuming the digest was 64-bit aligned, resulting in
misaligned memory accesses with armv7 ramdisk -Os bsd.rd ping
ok florian millert
----------

OK deraadt@

Use calloc(3) and recallocarray(3) instead of *alloc* + memset(0).

ok deraadt

SipHash_Final() was assuming the digest was 64-bit aligned, resulting in
misaligned memory accesses with armv7 ramdisk -Os bsd.rd ping
ok florian millert

New strstr() implementation from musl libc by Rich Felker.  This
version uses the two-way string matching algorithm and is faster
than the old implementation.  With this change, ports that check
for strstr having linear complexity time strstr will no longer
replace the libc strstr with a private version.
OK deraadt@ espie@

Prevent inosused from wrapping when soft updates is enabled while
scanning the used inode map.  The code as written assumes inosused
is signed but this is no longer the case.  OK deraadt@

isblank() is ANSI C since C99, no need to provide a replacement.
OK deraadt@

bluhm discovered "script < /dev/null" attempts tty operations in violation
of pledge.  We can wrap isatty() around those codepaths.
ok bluhm beck

Add comment what the test does.

RTM_PROTO3 messages should not trigger a resolv.conf check.

The pledge sigkill test is an outdated copy of sigabrt.  Remove the
former and activate the latter.
OK semarie@

Shuffle another function.

Add comment how the test works.

explicitly set the ownership on installed include files as well

Invoke install -d for each directory in the /usr/lib/clang hierarchy
as they aren't in mtree.  Problem with wrong ownership and permission
of directories reported by sthen@.

ok deraadt@ sthen@ tb@

Correct a format string

Problem noted by Michael W. Bombardieri (mb(at)ii.net)
ok mlarkin@ deraadt@

- Mention LIBCXX, prompted by espie@.

- Mention LIBCXX, prompted by espie@.

- Make it clear that CLANG_ARCHS, GCC3_ARCHS, GCC4_ARCHS refer to the base compiler.
Change "Clang 3.9.1" to just "Clang".

Ensure that the version part of $_url_base is correctly removed by
using $VNAME (x.y) instead of $VERSION (xy). This fixes the problem
that the version part ended up in installurl which is wrong anyway
and also confuses pkg_add.

Thanks to florian@ and trondd at kagu-tsuchi dot com for reporting
this.

OK tb@

sync

shorten introductory sentence and make deprecation clearer;
disgussed with deraadt@

Add SIOCATMARK to allow pledge("inet") programs to call sockatmark(3).
from Matthias Pitzl; OK deraadt@

Recognize break conditions and enter ddb if ddb.console is set.

ok visa@, deraadt@

Partially revert previous mallocarray conversions that contain
constants.

The consensus is that if both operands are constant, we don't need
mallocarray.  Reminded by tedu@

ok deraadt@

Shuffle route/interface changing functions together into kroute.c. Try to
group related functions in kroute.c together and comment them a bit.

No intentional functional change.

Revert ssl_asn1.c r1.50 - CBB and freezero(3) do not play nicely together.
Back this out while we investigate and implement a solution.

Found the hard way by sthen@

document more thoroughly the special status of modules gnu, imake, perl5
(for historical reasons)

okay aja@

Fold priv_write_file() into its only remaining user
priv_write_resolv_conf() and move the latter into kroute.c
with all its priv_ friends.

No intentional functional change.

Use freezero(3) for the imsg framework in imsg_free(3) and ibuf_free(3).

In our privsep model, imsg is often used to transport sensitive
information between processes.  But a process might free an imsg, and
reuse the memory for a different thing.  iked uses some
explicit_bzero() to clean imsg-buffer but doing it in the library with
the freezero() is less error-prone and also benefits other daemons.

OK deraadt@ jsing@ claudio@

Revise 'struct fpreg' and dump floating-point register in core dumps.  Also
reset the floating-point register state upon exec.

ok guenther@

Rework -L logic to use the idiom used in handling the leases file.
i.e. open FILE during program set up and use the FILE created for
the rest of the program lifetime after dropping privilege and
pledge()'ing. No need for passing messages to the priv process.

Tweak lease file handling a bit in passing.

Monitoring the -L file with external programs like sysutils/entr
still works.

Looks good to sthen@.

new X25519(3) manual page;
from Dr. Stephen Henson <steve@openssl.org>, OpenSSL commit d218f3c3

Use freezero() for the internal opaque structures, instead of the current
explicit_bzero()/free(). Less code and potentially less overhead.

Use freezero() for X25519 keys - same result with more readable code.

document three additional functions;
from Emilia Kasper <emilia at openssl dot org>, OpenSSL commit 4ac139b4

Rework and significantly extend TLS name verification tests to match
changes in libtls.

Rework name verification code so that a match is indicated via an argument,
rather than return codes. More strictly follow RFC 6125, in particular only
check the CN if there are no SAN identifiers present in the certificate
(per section 6.4.4).

Previous behaviour questioned by Daniel Stenberg <daniel at haxx dot se>.

ok beck@ jca@

sync

freezero() the key block; simpler code and less of it.

Use freezero() for i2d_SSL_SESSION() - one line of code instead of three.
In this case the memory allocated can also be significant, in which case
freezero() will have less overhead than explicit_bzero() (munmap instead
of touching all of the memory to write zeros).

Fix tabs in example code.

fix some .Xr errors that jmc@ found with mdoclint(1)

new manual page SSL_get_server_tmp_key(3)
from Matt Caswell <matt@openssl.org>, OpenSSL commit 508fafd8

Additional SSL_SESSION documentation
from Matt Caswell <matt at openssl dot org>, OpenSSL commit b31db505.
Improve crosslinking while here.

slaacdctl -> slaacctl;

Use __ASSEMBLER__ instead of __LANGUAGE_ASSEMBLY.
The latter is not defined by clang.

OK guenther@, kettenis@

Found another len += snprintf...
ok mikeb

sync

for pure *_ctrl() wrapper macros, move the reference from ssl(3)
to SSL_CTX_ctrl(3) to make ssl(3) slightly more palatable

Clean up disabled declaration in the text struct.

OK deraadt@

sync

Generate and install arm_neon.h on arm and arm64.

ok jsg@

The canonical name for ctl programs is without 'd'.
Pointed out by Brad.
OK deraadt@

new manual page SSL_CTX_set_tlsext_servername_callback(3) for SNI;
from <Jon dot Spillett at oracle dot com>
via OpenSSL commit 8c55c461