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

Check early if the mandatory carp "interface" was configured.

This allows the new -n config check to work correctly.

OK jsg@ deraadt@

Remove always false comparison: inosused type is ino_t, which is
unsigned.

While there, fix a whitespace issue.

OK deraadt@

tweak previous;

Convert various client key exchange functions to freezero(3). The memory
contents needs to be made inaccessible - this is simpler and less error
prone than the current "if not NULL, explicit_bzero(); free()" dance.

sync

Introducing freezero(3) a version of free that guarantees the process
no longer has access to the content of a memmory object. It does
this by either clearing (if the object memory remains cached) or
by calling munmap(2). ok millert@, deraadt@, guenther@

monir bump for freezero

Attempt to map msk(4) interrupt via MSI.

The device tree that ships with the overdrive 1000 has an interrupt-map
property that is known to be wrong.  Using MSI on msk makes the builtin
Ethernet on the overdrive 1000 work.

Tested on arm64 with
"Marvell Yukon 88E8059" rev 0x00, Yukon-2 Optima (0x1)

and i386 with
"Marvell Yukon 88E8072" rev 0x10, Yukon-2 Extreme rev. B0 (0x2)

Committing this early in the release cycle to try find cases where using
MSI doesn't work.

Based on part of an earlier patch from jmatthew@
ok jmatthew@ kettenis@

pasto; from <Jon dot Spillett at oracle dot com> via OpenSSL commit 3aaa1bd0

typo fix; from <Jon dot Spillett at oracle dot com>
via OpenSSL commit 7bd27895

Add a few missing quad-precision support functions on arm64 and reorder the
list to match what's in CMakeLists.txt.

ok sthen@

Sync symbol lists for trap/interrupt frame detection with what ddb(4) uses

ok deraadt@

Seven casts, a couple of tweaks and CFLAGS+=-Wsign-compare for the
win.

No intentional functional change.

malloc -> mallocarray; a typo

Convert some malloc(9) to mallocarray(9)

ok deraadt@

Convert a malloc(9) to mallocarray(9)

ok deraadt@

Convert a malloc(9) to mallocarray(9)

ok deraadt@

Convert a malloc(9) to mallocarray(9)

ok deraadt@

Convert some malloc(9) to mallocarray(9)

ok deraadt@

Convert some malloc(9) to mallocarray(9)

ok deraadt@

Convert some malloc(9) to mallocarray(9)

ok deraadt@

Use mallocarray to allocate multicast group memberships.

ok deraadt@

Correct wakeup() dance in sensor_task_work()
Problem noticed by krw

Simplify/clean up BUF_MEM_grow_clean().

ok beck@

With recallocarray() BUF_MEM_grow() is essentially the same as
BUF_MEM_grow_clean() (the only difference is clearing on internal down
sizing), so make it a wrapper.

ok beck@ deraadt@

Explicitly test for NULL.

ok beck@

Improve unknown protocol version handling.

Remove unused #define's and struct.

image/svg+xml is a default inbuilt media type.
Pointed out by Anton Lindqvist (anton.lindqvist AT gmail), thanks!

Fix multiple cases of reading past the end of a buffer in the sasyncd(8)
config parser found with afl.

feedback and ok millert@ ok deraadt@

snprintf() format string should be literal
avoid compiler silly warnings

sure deraadt@

format string is better be literal
OK deraadt

For legacy interrupt use the tag of the topmost bridge to establish the
interrupt.  We already correctly swizzle the pin.

ok patrick@

Bring over the changes I made to the armv7 version of this driver such that
interrupts are correctly routed to the boot cpu if that isn't the one
connected to CPU interface zero on the interrupt controller.

ok patrick@

re-enable POOL_DEBUG after the release; ok deraadt@

use .Em for emphasis, not .Pa

Reduce the overburden of signed vs unsigned comparisons by sprinkling
'int' -> 'unsigned int' (and visa versa) where obvious.

Steal a couple of 'unsigned' -> u_int32_t from reyk@'s dhcrelay
tweaks.

No intentional functional change.

change a log message from "warn" to "debug" level, as the condition it is
reporting is not actually a warning.

implement nonspecific EOI mode for the legacy PIC

ok deraadt

implement channels 1 and 2 of the legacy PIT.

ok otto, deraadt

Replace another snprintf() dance with easier to read code using
strlcat(). Shorter, clearer, fewer signed vs unsigned questions.

Use an 8K static buffer for pretty_print_classless() and use it
rather scribbling intermediate values into the final destination.

No intentional functional change.

Replace a mess of snprintf() dances with easier to read code using
strlcat(). Shorter, clearer, fewer signed vs unsigned questions.

Shrink static buffer for the string version of an option value from
32K to 8K. Since the string version of the entire lease is constructed
in a 8K buffer, bigger option values are pointless.

Use 8K of the saved space for a static buffer for pretty_print_string()
and use it rather scribbling intermediate values into the final
destination.

No intentional functional change.

Document the devel/meson MODULE.

Make network ports work on Shasta.

- localize the if, file and stat variables which also ensures that
  variables are not named like commands.
- change test from [] to [[]]

OK tb@ halex@

Sensors are run as callbacks inside tasks.  During suspend a sensor
could be running inside a driver that will be force-detached, or due
to tsleep end up disrupting the softstate/hardstate contract.  At
suspend time, quisce all these callbacks by waiting for completion.
This issue has never been observed for real, but may be implicated in
suspend/resume failures.
ok kettenis guenther mlarkin

Use ADDR64 opcodes to specify 64bit DMA addresses for all buffers.  This
consumes two ring entries per segment, halving the effective size of the
rings, but keeps things simple.  This is required for the onboard nic
on the Overdrive 1000 to work.

ok kettenis@, tested on i386 by jsg@

Remove some #if 0 code that dates back to r1.1

Pointed out by Michael W. Bombardieri

A pile of sizes to free(9).  In test for a few days in snapshots.
Errors will result in nice clean panic messages so we know what's wrong.
Reviewed by dhill visa natano jsg.

Two prototypes for acpi_maptable; merge to one place

Minimize differences in ifstart() function between netstart and
install.sub which makes it easier to spot changes in the future.

- comments and formatting
- quotes on assignments are not needed (netstart)
- remove stray space in test (netstart)
- use $file variable with while-loop (netstart)
- although valid, instead of i use $i in arithmetic test (install.sub)

OK krw@, tb@
Looks good deraadt@

Align comments of ifstart() function in netstart and install.sub.

Sync variable names with netstart version of stripcom().
Use $_file variable instead of $1 with the wile-loop.

Align comments of stripcom() function in netstart and install.sub.

Extend the information shown by diskinfo() to help to identify
disks. Extract the disk information enclosed in <> and the NAA
from the last matching dmesg line. Useful if there are multiple
identically sized disk of the same type.

Suggested by jirib at devio dot us
Discussed with deraadt@

In ssl.h TLS 1.0 is called TLSv1.  Adapt name in test to make it pass.
OK jsing@

Adapt test to new syslogd's local message priority.

Incoming TCP connections from clients fill the files of a log server.
A log client reconnects at every SIGHUP.  Write these accept and
close messages with debug priority, then they can be turned on in
syslog.conf.  Default is off.
While there, move a debug message and set the priority of the exit
message explicitly to error.
OK mpf@ millert@

Simply decoding of domain search option. No intentional functional
change.

Add prid for CN72xx/CN73xx.

Make SoC version available in a simple form.

Use uint8_t instead of u_int8_t - for consistency and to make things easier
for portable.

From Raphael Hittich.

si_addr should be of type void *, not char *

From Andrew Aldridge (i80and(at)foxquill.com)
ok millert@ mpi@

Simplify the size calculation for memset()

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

Inspired by recent dhcrelay(8) changes add some stricter CFLAGS. No code
changes needed (yet).

"kernel" got renamed to "boot" in vm.conf but I didn't commit the parse.y bits.

Found by Pontus Lundkvist

OK deraadt

replace some long if/else chains with a switch

a little const here and there to prevent rules from changing

prepenv can take a const rule

Remove the CD9660MAXPATH define. It was used to construct the path for
opening the file, so PATH_MAX makes more sense here. While there change
the code to do two less allocations per file.

ok deraadt

less chatty EXAMPLES; from anton lindqvist

trailing ; on end of macro definition is wrong; ok guenther

Do not expose vmm(4) VM IDs to the user, use vmd(8)'s IDs instead.

Each VM has two IDs: one from the kernel (vmm) and a different one
from userland (vmd).  The vmm ID is not consistent and incremented on
every boot during runtimg of the host system.  The vmd ID remains the
same during the lifetime of a configured VM, even after reboots.
Configured VMs will even get and keep their IDs when the configuration
is loaded.  This is more what users expect.

Pointed out and tested by otto@

OK deraadt@

Convert bcopy to memcpy where the memory does not overlap, otherwise,
use memmove.  While here, change some previous conversions to a simple
assignment.

ok deraadt@

shuffle for a saner read; help/ok bluhm

document -=; while here, simplify things so that we don;t add a separate
usage every time we think of a new way to use this;

-= bits from anton lindqvist
ok tb tom

Sizes for the remaining free() calls, and use mallocarray()
ok visa

Consistentcy between nmembers and size order. From Christopher Hettrick;
ok deraadt@

Check that local syslog messages have the the expected priority.

fix missing \ on \n, spotted by Edgar Pettijohn

Use the correct interrupt disestablish routine.

Extend the fdt interrupt API a little.

Add the LOG_SYSLOG facility to local messages.
OK millert@

Replace bcopy with a simple assignment where both variables are
properly aligned and sockaddr_union fields, or with memcpy when
the memory doesn't overlap.

OK bluhm@

use memset() instead of bzero()
OK jmatthew

fix format string found by clang -Wformat-security
OK deraadt millert

bump version for new development branch

Compile C code with -funwind-tables.  Fixes exception handling on architectures
that don't generate .eh_frame info by default such as arm64.

ok jsg@

first print size in meta-data then supplied arg size when an inconsistency is
detected wrt recallocarray()

remove stray character in previous that broke the build

Unify a few attach-time patterns between usb *com drivers, and remove
extra zero'ing of variables not needed because softc is pre-zero'd.
ok jsg

add sizes to free() calls
ok dhill

Convert bcopy to memcpy as the memory does not overlap.

ok deraadt@

3 more mallocarray() uses

Syslogd's debug and error messages have changed a bit, adapt test.

Replace 2 bcopy()'s with a simple assignment as both variables are
properly aligned malloc(9)d data and sockaddr_union fields.  While here,
convert the remaining bcopy() to memmove().

with and ok @bluhm

The global variable Startup is not used anymore and can be deleted.
The functionality has moved into log_setdebug().
OK millert@