Pull up following revision(s) (requested by tsutsui in ticket #1026):

external/mit/xorg-server.old/dist/hw/netbsd/x68k/x68kInit.c: revision 1.3

Use AllocDevicePair() to initialize input devices in InitInput().

This should have been done on the initial X11R7'fied imoprt as
upstream xnest did:
https://cgit.freedesktop.org/xorg/xserver/commit?id=32ce5c83a504d2cafd2b19ed628b40032ef347b3

Tested and no visible regression on XM6i.

(martin)

Note support for TI AM335x SoC

(jmcneill)

make(1): add test for .MAKE.SAVE_DOLLARS

(rillig)

Pull up following revision(s) (requested by jdolecek in ticket #1025):

sys/dev/wsfb/genfb.c: revision 1.73

reduce stack usage in genfb_calc_hsize()

(martin)

Pull up following revision(s) (requested by jdolecek in ticket #1024):

sys/dev/pci/pci_subr.c: revision 1.224

change pci_conf_print() to allocate memory for the regs dynamically
instead of on-stack

(martin)

Pull up following revision(s) (requested by roy in ticket #1023):

external/apache2/mDNSResponder/dist/mDNSShared/PlatformCommon.c: revision 1.6
external/apache2/mDNSResponder/dist/mDNSPosix/mDNSPosix.c: revision 1.17
external/apache2/mDNSResponder/dist/mDNSPosix/PosixDaemon.c: revision 1.13
external/apache2/mDNSResponder/dist/mDNSPosix/PosixDaemon.c: revision 1.14

mdnsd: Treat EADDRNOTAVAIL as a transient error

mdnsd: starting and stopping are informational messages

mdnsd: Make the unable to parse resolv.conf message informative

(martin)

make(1): fix missing error message about missing @ delimiter

This had been broken since 2020-07-03, during a "refactoring".

(rillig)

make(1): add test about missing delimiters in :@ modifier

These error conditions have been broken since var.c 1.236 on 2020-07-03.

(rillig)

share/mk/bsd.README: fix typo

(rillig)

style: fix typo about enum constants being capitalized

(rillig)

make(1): remove references to the removed lst.lib

(rillig)

Refactor remaining mount_* commands to use the common pathadj()
function for resolving paths.

Make pathadj() no longer warn about symlinks. Symlinks in /dev are
regularly used in several places like LVM . The warning was also
only visible when calling a mount_* command directly as mount(8)
itself would resolve the path witout warning before passing it to
a mount_* command.

(mlelstv)

#define<tab>
Nuke trailing whitespace.

(simonb)

Rework "machine cp0" command and support macros to use CP0 reg defines
instead of magic numbers for CP0 regs with a select number.

(simonb)

Add CP0 Config Registers 6 and 7.

(simonb)

Use EIMR/EIRR regs definitions from <mips/cpuregs.h>

(simonb)

Adjust for new CP0 reg names, comment out most of the Cavium CP0
specific functions that are unused.

(simonb)

Remove mostly duplicate MIPS spec CP0 regs from octeon_corereg.h, move
the Cavium specific CP0 regs to <mips/cpuregs.h> as done for other core
specific regs.

(simonb)

Explicitly initialize origColormapValid for readability.

(tsutsui)

add support swp,swpb instruction emulation

(ryo)

- add support conditionally execution for A32 instruction emulation
- separated the processing of ARM and THUMB emul clearly. do not confuse the Thumb-32bit instruction with the ARM instruction.
- use far_el1 instead of tf_pc to return correct fault address when instruction emulation

(ryo)

make(1): replace macros with functions

(rillig)

Implement functions to restore palette settings on exiting Xserver.

(tsutsui)

Add prototype declarations for CG2 functions.

(tsutsui)

make(1): condense the list library into a single file

The list library is only used in make(1). Having it spread out over 28
files made it look more complex than it really is. In fact, it's just a
versatile generic data type like in hash.c.

Having all the list functions in a single file reduces the code size,
both by omitting the many RCS Ids and by inlining commonly used code.

(rillig)

Add a space in a comment.

(simonb)

Give syspkg name to Xsun server files.

(tsutsui)

Add /usr/tests/sys/crypto/chacha to etc/mtree/NetBSD.dist.tests.

(riastradh)

Ensure aes_ccm module init runs after aes module init.

Otherwise the AES implementation might not be selected early enough.

(riastradh)

Fix more sort order.

(riastradh)

Add missing aes_ccm.c, aes_ccm_mbuf.c.  Fix sort order.

(riastradh)

Simplify internal Poly1305 API in adiantum.c.

Should be slightly faster this way too.

(riastradh)

Add chacha to rump libcrypto.

(riastradh)

pull in a bit more FreeBSD code to allow specifying truncation of
the regular bmap (IO_NORMAL) independently of the extattr bmap (IO_EXT).
fixes fs corruption when removing extattrs in UFS2.

(chs)

skip the assertions about page-locking when allocating to the extattr bmap,
since extattrs do not use the page cache.

(chs)

Start teaching sh3 code about STX7105.

Kernel option STX7105 to select CPU product (TODO: all of the options
that select CPU product should be defflag'ed to opt_cputype.h).

The ST40 cache sizes can be customized for each product.  For now just
hardcode the STx7105 values in the switch, but may be they should be
kernel options.

(uwe)

Fix typo in comment; match the paper's notation.

No functional change.

(riastradh)

Define CPU_PRODUCT_STX7105.

I'm not sure if this should rather be named CPU_PRODUCT_ST40_300, but
that's probably too general.  These constants don't have to be
backward compatible, so we can re-do this properly later if we need to.

(uwe)

Add kernel ChaCha test to exercise all available implementations.

(riastradh)

Implement ChaCha with NEON on ARM.

XXX Needs performance measurement.
XXX Needs adaptation to arm32 neon which has half the registers.

(riastradh)

Implement ChaCha with SSE2 on x86 machines.

Slightly disappointed that it only doubles, rather than quadruples,
throughput on my Ivy Bridge laptop.  Worth investigating.

(riastradh)

Convert crypto/adiantum to use new ChaCha API.

(riastradh)

New ChaCha API in kernel.

This will enable us to adopt MD vectorized implementations of ChaCha.

(riastradh)

Add some Intel intrinsics for ChaCha.

_mm_load1_ps
_mm_loadu_si128
_mm_movelh_ps
_mm_slli_epi32
_mm_storeu_si128
_mm_unpackhi_epi32
_mm_unpacklo_epi32

(riastradh)

Fix target attribute on _mm_movehl_ps, fix clang _mm_unpacklo_epi64.

- _mm_movehl_ps is available in SSE2, no need for SSSE3.
- _mm_unpacklo_epi64 operates on v2di, not v4si; fix.

(riastradh)

Nix outdated comment.

The substance of the change that introduced it was reverted, but I
neglected to revert the comment when reverting the substance.

(riastradh)

Add 32-bit load, store, and shift intrinsics.

vld1q_u32
vst1q_u32
vshlq_n_u32
vshrq_n_u32

(riastradh)

Fix missing clang big-endian case.

(riastradh)

Make aes boot message verbose-only.

(riastradh)

Note dependency of adiantum on aes.

Forgot this a while back.

(riastradh)

Omit useless AES call.

This must have been a vestige from editing that I never got around to
removing, oops.  Should speed up adiantum encryption a wee bit!

(riastradh)

Remove now-unused legacy rijndael API.

(riastradh)

Make this build with or without options IPSEC.

Not really that useful without options IPSEC, but simply uncommenting
mvxpsec in conf/ARMADAXP didn't build, and this change is trivial, so
why not.

(riastradh)

Omit needless rijndael dependencies.

(riastradh)

Remove now-needless AES-CCM fallback logic.

These paths are no longer exercised because all of the aes_impls now
do the AES-CCM operations.

(riastradh)

Implement AES-CCM with NEON.

(riastradh)

Implement AES-CCM with ARMv8.5-AES.

(riastradh)

Invert some loops to save a branch instruction on every iteration.

(riastradh)

Implement AES-CCM with VIA ACE.

(riastradh)

Implement AES-CCM with SSSE3.

(riastradh)

Implement AES-CCM with SSE2.

(riastradh)

Implement AES-CCM with x86 AES-NI.

(riastradh)

Implement AES-CCM with BearSSL's bitsliced 32-bit aes_ct.

(riastradh)

Push CBC-MAC and CCM block updates into the aes_impl API.

This should help reduce the setup and teardown overhead (enabling and
disabling fpu, or expanding bitsliced keys) for CCM, as used in
802.11 WPA2 CCMP.  But all the fiddly formatting details remain in
aes_ccm.c to reduce the effort of implementing it -- at the cost of a
handful additional setups and teardowns per message.

Not yet implemented by any of the aes_impls, so leave a fallback that
just calls aes_enc for now.  This should be removed when all of the
aes_impls provide CBC-MAC and CCM block updates.

(riastradh)

Convert malloc -> kmem.

Switch order of members for better alignment.  Sort includes.

(riastradh)

Definitions for ST40 Privileged Mapping Buffer.

(uwe)

Convert ieee80211_crypto_ccmp.c to new aes_ccm API.

This will make it easier to provide better hardware acceleration
without fpu enabling/disabling overhead for each block of data.

(riastradh)

New aes_ccm API.

Intended for use in net80211 for WPA2 CCMP.

(riastradh)

Split aes_cbc_* and aes_xts_* into their own header files.

aes.h will remain just for key setup; any particular construction using
AES can have its own header file so we can have many of them without
rebuilding everything AES-related whenever one of them changes.

(Planning to add AES-CCM and AES-GCM too.)

(riastradh)

Split aes_impl declarations out into aes_impl.h.

This will make it less painful to add more operations to struct
aes_impl without having to recompile everything that just uses the
block cipher directly or similar.

(riastradh)

Invert some loops to save a jmp instruction on each iteration.

No semantic change intended.

(riastradh)

Tweak VIA CPU RNG.

- Cite source for documentation.
- Omit needless kpreempt_disable/enable.
- Explain what's going on.
- Use "D"(out) rather than "+D"(out) -- no REP so no register update.
- Fix interpretation of number of bytes returned.

The last one is likely to address

[  4.0518619] aes: VIA ACE
....
[  11.7018582] cpu_rng via: failed repetition test
[  12.4718583] entropy: ready

reported by Andrius V.

(riastradh)

remove duplicate, noted by chuq (this was never used).
perhaps either move extattr.c from generic here, or move the man page
extattr.3 in gen?

(christos)

make(1): add newly added unit tests

(rillig)

make(1): add tests for previously uncovered code

(rillig)

make(1): make it easy to run gcov on the code

There seems to be no gcov support in share/mk yes, but it's still good
to have, especially for a complex program like make(1).

(rillig)

make(1): indent Makefile directives like in pkgsrc

This makes it easier to see the corresponding .if/.endif, even without
comments.

(rillig)

make(1): format Makefile consistently

(rillig)

make(1): regroup source files

(rillig)

make(1): add test for undefined (or empty) variable in :? modifier

(rillig)

make(1): add test for brk_string with more than 50 words

(rillig)

upgrades to upgrade instructions

(nia)

evbmips: add ofctl(8) and /dev/openfirm support

(jmcneill)

make(1): remove redundant condition

If there are multiple words from brk_string, none of them can be empty.
And if there is oneSingleWord that is empty, it doesn't hurt to add 0
bytes.

(rillig)

make(1): prefer direct jump over indirect variable assignment

(rillig)

make(1): make condition in ModifyWord_SubstRegex simpler

The generated code is still the same, at least with Clang.

(rillig)

make(1): reduce lifetime of regmatch_t for :C modifier

(rillig)

make(1): rename local variable

(rillig)

make(1): allocate capturing groups for :C modifier statically

Since there are at most 10 capturing groups, it's easier to allocate them
on the stack.

To avoid growing the code size on x86_64, the matches have been moved to
the end of the struct, to keep the other offsets small.

(rillig)

make(1): clean up Var_Export

(rillig)

make(1): inline Var_Parse_State into ApplyModifiersState

There was no need to have this as a separate struct.  Especially none of
the modifiers used by ModifyWords modify this state, therefore it was
not necessary to pass it by reference.  This makes the code easier to
understand since there's less modifiable state.

(rillig)

make(1): document ApplyModifiersState.cp

(rillig)

make(1): eliminate ApplyModifiersState.tstr

This field always pointed to the beginning of the current modifier.
Therefore a better name is "mod", and there is no need to store it in the
shared state.

(rillig)

<xen/xenio.h> is in fact used by the newly imported xentools 4.13,
reinstantiate it

header is for use by xentools only, which define domid_t themselves,
so it should not be a problem the header doesn't define it per PR port-xen/52874

(jdolecek)

Replace the */ I accidentally removed in the last commit

(skrll)

Use proper args for dixLookupResourceByType() to get defcolormap.

Botched in mechanical 1.20 updates.

(tsutsui)

Explicitly disable dbe, record, and present DIX extentions.

(tsutsui)

Apply upstream "free the EQ allocated memory on shutdown" fixes.

This should be updated before 1.20 import:
https://cgit.freedesktop.org/xorg/xserver/commit/?id=87d4f90bfcb509471ac9e7886e14a92b33223fd7

(tsutsui)

make(1): only set missing_delim if it is actually missing

Just to make it easier to understand the code.

(rillig)

make(1): fix wrong warning about missing delimiter

(rillig)

make(1): demonstrate wrong error message about missing delimiter

The current practice of setting st->delim at the beginning of each
modifier and resetting it again at the end produces too many error
messages.  In this case, there is no missing delimiter.

(rillig)

make(1): reduce code size on x86_64

(rillig)

unifdef -U_LKM

(skrll)

Trailing whitespace

(skrll)

unifdef -U_LKM

(skrll)

unifdef -U_LKM

(skrll)

unifdef -U_LKM

(skrll)

unifdef -U_LKM

(skrll)

unifdef -U_LKM

(skrll)

Trailing whitespace

(skrll)

Trailing whitespace

(skrll)

unifdef -U_LKM

(skrll)

unidef -U_LKM

(skrll)

Use proper ANSI offsetof(3) to specify framebuffer offset in struct.

Fixes build error on sparc64.  No binary change on sun3.

(tsutsui)

Move machine-specific fixes into separate functions to improve readability.

(jdc)

Add a comment to CACHE_LINE_SIZE / COHERENCY_UNIT size defines

(skrll)

freescale support in GENERIC

(nia)

more 9.0 hardware

(nia)

Reduce the window of having interrupts disabled in cpu_switchto{,_softint}
and ensure astpending is checked with interrupts disabled.

(skrll)

On second thoughts this can't be conditional so define CACHE_LINE_SIZE /
COHERENCY_UNIT as 128 for all mips.

(skrll)

Define CACHE_LINE_SIZE / COHERENCY_UNIT as 128 for MIPS64_OCTEON

(skrll)

fix build with llvm/clang.

(ryo)

fix build:
- add .../xorg subdir to the path
- add dbe and present extensions, both wanted via linkage

.. but maybe these shouldn't be built?  they're not in sets.

(mrg)

Add .debug binaries for Xsun servers.

Note daily build.sh on releng.netbsd.org has MKDEBUG=yes
so local test builds should also include it.

(tsutsui)

Remove duplicated (and .if 0'ed out) ${XSERVER_XFREE86} checks.

(tsutsui)

Remove definitions for Xdreamcast, Xhpc, Xmacppc, and Xnewsmips.

All these port specific X11R6 servers just used MI wscons, and
all of them have been switched to Xorg servers with wsfb driver etc.
Even if someone wants a smaller monolithic server, it should be
written as a MI "Xwscons" server.

(tsutsui)

Don't build Xsun servers for sparc and sparc64.

Not tested, and maybe not worth for wscons'fied ports.

(tsutsui)

move $VERSION from Makefile.inc into the single Makefile that uses it.

this should do two nice things:
- eliminate "nbsed" missing messages in builds
- slightly speed up the build by removing a few dozen exec sed calls

(mrg)

Reorganize CPPFLAGS.

- use ${X11INCS.DIX} in <bsd.x11.mk>
- explicitly undef HAVE_XORG_CONFIG_H to avoid reference to
  hw/xfree86/common in mi/miinitext.c
- remove -DHAVE_DIX_CONFIG_H which is already defined in
  ${X11FLAGS.DIX} and pulled via Makefile.servermod

XXX: -DHAVE_STRCASECMP should also be moved to ${X11FLAGS.DIX},
    or should be pulled via include/dix-config.h?

(tsutsui)

Normalize #include paths.

(tsutsui)

Note about sun3 Xsun servers.

(tsutsui)

Add build glue for Xorg-Server-1.20'fied monolithic Xsun servers.

(tsutsui)

Import WIP Xorg-Server-1.20'fied monolithic Xsun servers.

This is based on 1.10 version imported into xorg-server.old and
all upstream API changes between xorg-server 1.10 and 1.20 are
applied almost mechanically.
https://github.com/tsutsui/xorg-server-Xsun/commits/xorg-server-1.20

Xsun and XsunMono servers are also confirmed working with bwtwo on
3/60 and tme, and cgtwo on tme. XKB stuff is still to be resolved.

(tsutsui)

enable -Walloca, warn if something uses alloca()

(jdolecek)

Add build glue files for Xorg-Server-1.10'fied monolithic Xsun servers.

Not enabled and just for reference.

(tsutsui)

Import WIP Xorg-Server-1.10'fied ancient monolithic Xsun servers.

There are still several issue especially around XKB stuff,
but both Xsun and XsunMono servers are confirmed working with
bwtwo on 3/60 and tme, and also cgtwo on tme.
See my port-sun3@ posts for more details:
https://mail-index.netbsd.org/port-sun3/2020/07/17/msg000157.html

Note a newer Xorg Server 1.20 based version is also ready
so these 1.10 sources are imported as referenece for people
who will try to port other X11R6 servers.

(tsutsui)

mdnsd: Make the unable to parse resolv.conf message informative

resovconf will SIGHUP mdnsd when resolv.conf changes so this message
should not be an error.

(roy)

Note openresolv update

(roy)

Note the new resolvconf files

(roy)

openresolv: Rework the build system to cope with more directories

While here, install avahi-daemon and mdnsd notifiers for when
/etc/resolv.conf is updated.

(roy)

bwfm: Switch from pcq to pool_cache.

pcq_get is required to be serialized, but it's far from clear that it
is serialized here.

(riastradh)

Sort includes.  Nix trailing whitespace.

No functional change intended.

(riastradh)

Need <sys/kmem.h> for kmem_*.

Currently accidentally side-loaded by <sys/pcq.h>.

(riastradh)

Add include guards and appropriate includes to bwfmreg.h, bwfmvar.h.

No functional change intended.

(riastradh)

Sort #includes.  Nix trailing whitespace.

No functional change intended.

(riastradh)

Sort #includes.  Nix trailing whitespace.

No functional change intended.

(riastradh)

Omit needless <sys/pcq.h>.

(riastradh)

Split the local disk availability step into two phases to allow scripts
that pre-populate parts of the system (e.g. a tmpfs based /var) an
easy place to plug in like:

# REQUIRE: mountcritlocal
# BEFORE: MOUNTCRITLOCAL

This also cleans up the existing special handling a bit by separating it
into new scripts. All later scripts now depend on MOUNTCRITLOCAL.
Discussed on tech-userlevel some time ago.

(martin)

Initialize PageMask and Wired registers on secondary processors.

(jmcneill)

Handle IPI_KPREEMPT

(jmcneill)