Regen.

(msaitoh)

Simplify descriptions of Snow Ridge internal Ethernet devices.

(msaitoh)

viadrmums(4): build legacy VIA DRM UMS driver module for amd64.

This driver is not built-in by default, thus loadable module can help (un)lucky
owners of 64-bit capable VIA (Nano/Eden) systems or early AMD/Intel systems
with some VIA chipsets, which include VIA integrated graphics.
I also boldly added product IDs for few later models from VX8xx/VX9xx chipsets
without 3D support (DX9_0) to "expand" the driver support to more systems.
Tested successfully basic functionality on VX800, and partially successfully
on VX900 (on VX900 Xorg failed to initialize due to openchrome related issues,
viadrmums attaches and it is by used the driver).
Didn't test on VX855, I don't have one.

Pull up to netbsd-10 is needed.

(andvar)

xvif(4): Omit needless membars in xennetback_connect.

xneti is a private data structure to which we have exclusive access
here; ordering the stores doesn't make sense.

(riastradh)

xvif(4): Omit needless membars in xennetback_rx_copy_process.

- No need for barrier around touching req_cons and rsp_prod_pvt,
  which are private.

- RING_PUSH_RESPONSES_AND_CHECK_NOTIFY updates the shared req_prod and
  then issues xen_mb, which is all that we need between the update of
  shared req_prod and hypervisor_notify_via_evtchn.

  (Between updating the shared req_prod and issuing
  hypervisor_notify_via_evtchn, only xen_wmb is needed.  But after
  writing to the shared req_prod, RING_PUSH_REQUESTS_AND_CHECK_NOTIFY
  must also read from the shared rsp_event, which requires the
  store-before-load ordering that only xen_mb provides.)

(riastradh)

xvif(4): Simplify while loop in xennetback_evthandler.

No functional change intended.

(riastradh)

xvif(4): Omit needless membars in xennetback_evthandler.

This should improve throughput without any impact on correctness.

(riastradh)

xvif(4): Move expensive xen_mb out of xennetback_evthandler loop.

Use the cheaper RING_HAS_UNCONFIRMED_REQUESTS for most of the loop.

This should improve throughput without any impact on correctness.

(riastradh)

xvif(4): Omit local variable aliasing xneti->xni_txring.req_cons.

No functional change intended.

(riastradh)

xvif(4): Add missing xen_rmb in xennetback_evthandler.

(riastradh)

xvif(4): Comment on memory barriers in xennetback_evthandler.

Note which ones appear unnecessary and which ones appear too strong,
but don't change them.

No functional change intended.

(riastradh)

workqueue(9): Factor out wq->wq_flags & WQ_FPU in workqueue_worker.

No functional change intended.  Makes it clearer that s is
initialized when used.

(riastradh)

workqueue(9): Sort includes.

No functional change intended.

(riastradh)

workqueue(9): Avoid unnecessary mutex_exit/enter cycle each loop.

(riastradh)

workqueue(9): Stop violating queue(3) internals.

(riastradh)

workqueue(9): Sprinkle dtrace probes for workqueue_wait edge cases.

Let's make it easy to find out whether these are hit.

(riastradh)

workqueue(9): Avoid touching running work items in workqueue_wait.

As soon as the workqueue function has called, it is forbidden to
touch the struct work passed to it -- the function might free or
reuse the data structure it is embedded in.

So workqueue_wait is forbidden to search the queue for the batch of
running work items.  Instead, use a generation number which is odd
while the thread is processing a batch of work and even when not.

There's still a small optimization available with the struct work
pointer to wait for: if we find the work item in one of the per-CPU
_pending_ queues, then after we wait for a batch of work to complete
on that CPU, we don't need to wait for work on any other CPUs.

PR kern/57574

XXX pullup-10
XXX pullup-9
XXX pullup-8

(riastradh)

workqueue(9) tests: Add test for PR kern/57574.

XXX pullup-10
XXX pullup-9
XXX pullup-8

(riastradh)

workqueue(9) tests: Destroy struct work immediately on entry.

(riastradh)

workqueue(9) tests: Nix trailing whitespace.

(riastradh)

tests/rump/rumpkern: Use PROGDPLIBS, not explicit -L/-l.

This way we relink the t_* test programs whenever changes under
tests/rump/kernspace change libkernspace.a.

(riastradh)

sqlite3/lib/Makefile: -Wno-error=restrict is a gccism.

Let's try to get at least one working clang autobuild this summer,
shall we?

(riastradh)

libc/resolv/res_debug.c: Minor whitespace fixes.

(riastradh)

Regen.

(msaitoh)

Add some Intel Xeon D-2100 devices. Fix description of Intel 0x37d0.

(msaitoh)

lint: in -a mode, do not warn about integer conversions from 'int'

Since tree.c 1.552 from 2023-07-08, lint warned about integer
conversions from 'int' or 'unsigned int' to smaller integer types.  This
only affected 32-bit platforms where size_t is 'unsigned int' rather
than 'unsigned long', as on these platforms, the integer ranks of 'int'
and 'long' are the same, see INT_RANK in inittyp.c.

Discovered by lib/libkvm, which fails on i386 when lint generates any
warnings.

(rillig)

tests/lint: test integer conversions on ilp32 int platforms

(rillig)

Avoid adding another member to the softc and use sc_flags instead.

NFCI.

(nat)

Add a flag for output only devices and attachments.

It is necessary to skip the test for the device as output only attached
devices lack the ability for the device to be probed - such as the 1602 lcd
module.

(nat)

Add a detach function.

(nat)

The analysis documented in PR misc/56990 is correct.
Fix by not returning when encountering a ruleset rule.

The code up to now would stop at any group rule.

ruleset rules are marked as group rule and a dynamic rule.

processing is only finished when a result is present AND
we are looking at a plain group rule.

(kardel)

Remove trailing tabs.

(tsutsui)

Specify options "AutoAddDevices" to prefer xorg.conf keyboard options.

Fixes PR/57346.
Should be pulled up to netbsd-10.

(tsutsui)

traceroute/Makefile: Nix trailing whitespace.

(riastradh)

gcc/README.warnings: Nix trailing whitespace.

(riastradh)

t_cdb: No need for weird padding any more.

cdbw_output never needed it at runtime, and the declaration no longer
makes gcc angry about not having it.

(riastradh)

libnpf(3): No need for weird padding any more.

cdbw_output never needed it at runtime, and the declaration no longer
makes gcc angry about not having it.

(riastradh)

npftest(8): No need for weird padding any more.

cdbw_output never needed it at runtime, and the declaration no longer
makes gcc angry about not having it.

(riastradh)

dev_mkdb(8): No need for weird padding any more.

cdbw_output never needed it at runtime, and the declaration no longer
makes gcc angry about not having it.

(riastradh)

services_mkdb(8): No need for weird padding any more.

cdbw_output never needed it at runtime, and the declaration no longer
makes gcc angry about not having it.

(riastradh)

cdbw(3): Make cdbw_output descr parameter type less confusing.

This is a string of _up to_ 16 bytes, used with strncpy(..., 16).
Specifying `const char descr[16]', while formally equivalent to
`const char *descr' in standard C, now provokes the ire of gcc when
the caller does not provide a buffer of at least 16 bytes.

(riastradh)

nix the NetBSD specific GEM_BUG_ON().

avoids GCC 12 warnings, and matches upstream closer.

(mrg)

comment a function that has a clear overbounds read but it isn't used.

found by GCC 12.

(mrg)

ensure all data passed to copyout() has been initialised.

found by GCC 12.

(mrg)

update sparc asan issue with details.

(mrg)

use standard strncpy() idiom to completely zero a buffer, including
explicitly nul the final char.

found by GCC 12.

(mrg)

avoid uninitialised variable accesses.

if __kernel_rem_pio2() or __kernel_rem_pio2f() are called with "nx" less
than 2, the local variable fq[0] may be accessed uninitialised.

__kernel_rem_pio2() has direct calls with nx = 1, and __kernel_rem_pio2f()
is called with a value starting at 3, but may be decreased to less than 2,
implied by this code , if not actually avoided by the tx[] setup above:
nx = 3;
while(tx[nx-1]==zero) nx--;    /* skip zero term */
n  =  __kernel_rem_pio2f(tx,y,e0,nx,2,two_over_pi);

found by GCC 12.

(mrg)

introduce new GCC 12 warning disables and use them in a few places

this introduces 4 new warning disable flags:

  CC_WNO_MISSING_TEMPLATE_KEYWORD
  CC_WNO_REGISTER
  CC_WNO_STRINGOP_OVERREAD
  CC_WNO_ARRAY_BOUNDS

and documents them in README.warnings.  of these, the string op
and array bounds are both problematic (real bugs) and also spurious
(not real bugs), and the other 2 are mostly temporary for older
3rd party code.

add some new uses of CC_WNO_STRINGOP_OVERFLOW.

fix m68k build for gallium and GCC 12.

(mrg)

lists: Fix build with MKGCCCMDS=no && MKDEBUGLIB=yes

(rin)

fix array vs pointer function declaration.

also, in some callers, and make sure to provide all the accessed
backing for a string array.

found by GCC 12.

(mrg)

put amd64 back to GDB 11.  it doesn't build for me, or others.

the first problem is that this rule:

GDBvn.texi: ${DIST}/gdb/version.in
echo "@set GDBVN $$(${TOOL_CAT} ${.ALLSRC})" > ${.TARGET}

conflicts with the "GDBvn.texi" in the source tree and fail to write
this file with r/o source trees.

the second problem is that gdbserver fails to link because it compiles
the wrong file to create target.o.  this seems like a very bad make or
bsd.*.mk bug -- "SRCS= .. target.cc ...", and yet, make manages to
compile the file "target.c" to create target.o, and then the required
symbols the rest of gdbserver needs are missing.

the third problem is that when you make it build the right target.cc,
it wants bfd.h, and gmp.h, and even after solving those issues, i'm
still getting a fourth issue linking gdbserver and thus reverting.

(mrg)

libm: Add fma(3) and friends to m68k

(rin)

remove always-true part of condition.

found by GCC 12.

(mrg)

avoid uninitialised variable.

found by GCC 12.

(mrg)

fix mis-matched function prototype and definitions.

found by GCC 12.

(mrg)

fix indentation issues.

found by GCC 12.

(mrg)

fix potentially uninitialised data being used.

found by GCC 12.

(mrg)

fix always true conditional by removing the address-of operator.

found by GCC 12.

(mrg)

tests/lint: show that portable mode depends on PTRDIFF_TSPEC

Since 2023.07.08.12.45.43, lint warns in lib/libkvm on i386.

(rillig)

rpcgen: don't pass length of source to string copy operation

Altough the prior code can't fail, GCC complains about the practice.

(tnn)

makemakedb: don't return uninitialized token length if stemming fails

(tnn)

services_mkdb: pad argument to cdbw_output(3) to match it's prototype

(tnn)

tail: adjust misleading indentation in macro. NFC.

(tnn)

style(5): Advise against new struct typedefs and explain why.

Proposed on tech-kern:
https://mail-index.netbsd.org/tech-kern/2023/07/11/msg028950.html

Positive feedback to general concept, negative feedback to specifics
and phrasing of the first iteration but no objections to latest
iteration after several weeks at:
https://mail-index.netbsd.org/tech-kern/2023/07/16/msg028994.html

(riastradh)

Prevent us from using the phony_iconv_open(). Our iconv_open does not take
"wchar_t" as an argument, so define __STDC_ISO_10646__

(christos)

regen

(christos)

Add missing i386 tdeps

(christos)

radeon: Suspend ioctls while device is suspended.

XXX pullup-10

(riastradh)

nouveau: Suspend ioctls while device is suspended.

XXX pullup-10

(riastradh)

amdgpu: Suspend ioctls while device is suspended.

XXX pullup-10

(riastradh)

distrib/sets/lists: Fix libtsan entries.

- No obsolete .so.N or .so.N.M entries.
- libtsan.so for gcc.
- libtsan.so.1* for gcc=10.
- libtsan.so.2* for gcc=12.
- No libtsan.so.1* on aarch64, libtsan on aarch64 is new in gcc12.

(riastradh)

fix config.h confusion

(christos)

netbt(4): Initialize bt_lock earlier.

Use a driver-class module modcmd init function, instead of a socket
domain init function; the socket-domain ones don't run until after
configure, but we need this to be initialized before configure so
that Bluetooth HCI drivers like ubt(4) can use it.

This is suboptimal but it's the least intrusive way I've thought of
to get this working, even if it's a little grody to make netbt a
`driver-class' (builtin) module.  Note that this doesn't mean netbt
becomes dynamically loadable or unloadable; we're just using a module
for initialization ordering.

PR kern/56988

XXX pullup-10

(riastradh)

sys/lwp.h: Slightly more paranoia re curlwp in PR port-evbarm/57564.

(riastradh)

sys/lwp.h: KASSERT -> KASSERTMSG

Might help diagnose PR port-evbarm/57564.

(riastradh)

Update /proc/cpuinfo.

- Move "ssbd" to an unused Linux mapping.
- Update unused Linux mappings.

(msaitoh)

libm: Add dummy remainderl and remquol.

These are pretty bad -- these aren't transcendental functions; not
rocket science to make them correctly rounded -- but let's just make
sure they're available in libm for netbsd-10.

XXX pullup-10

(riastradh)

rnd(4): Document `entropy: best effort' in random(4).

(riastradh)

ichsmb(4),ismt(4): Add Snow Ridge support.

(msaitoh)

Fix detection of availability of MSI/MSI-X on some systems.

Try to find all functions on bus 0, device 0 to find a PCI host bridge.
Some CPU's host bridge is at 0:0.4. Tested by Intel Snow Ridge.

(msaitoh)

sys/crypto: aarch64: Catch up with builtin rename for GCC12

Kernel self tests successfully pass for aarch64{,eb}.

Same binary generated by GCC10 and GCC12 for:
---
#include <sys/types.h>
#include "arm_neon.h"

uint32x4_t my_vshrq_n_u32(uint32x4_t v, uint8_t bits)
{
return vshrq_n_u32(v, bits);
}

uint8x16_t my_vshrq_n_u8(uint8x16_t v, uint8_t bits)
{
return vshrq_n_u8(v, bits);
}
---

(rin)

sys/crypto: Introduce arch/{arm,x86} to share common MD headers

Dedup between aes and chacha. No binary changes.

(rin)

sys/crypto/{aes,chacha}/arch/arm/arm_neon.h: Sync (whitespace fix)

No binary changes.

(rin)

t_asan_global_buffer_overflow: Avoid ODR Violation for pic variants

Common symbol triggers ODR (One Definition Rule) Violation correctly,
instead of Global Buffer Overflow.

XXX
Add test for odr_violation.

(rin)

lists/m68k: Obsolete gcc-9 headers

(rin)

lists/aarch64: Obsolete gcc-9 headers

(rin)

openssh: channel_new(): Appease GCC12 -Wmaybe-uninitialized for some archs

IIUC, ``found'' is always initialized. Seems like GCC bug.

(rin)

README.gcc12: Updated aarch64, arm, i386, m68k, powerpc, and sh3

aarch64{,eb}:
- Everything (without x11 yet) works just fine, except for libtsan
  (not a regression, this is newly introduced to aarch64 for GCC12).

earmv5{,eb}:
- As far as I can see, everything (nox11) seems OK.
- Full ATF is on-going.

earmv[67]hf{,eb}:
- Everything (nox11) works just fine.

i386:
- lib*san requires 64-bit atomic ops. If they are built with -march=i586,
  all tests in ATF pass. Alternatively, we can probably use 32-bit atomic
  variables instead, with some restrictions (now examining).
- New kernel freeze observed during full ATF run.

m68k:
- Another -fstack-protector breakage.
- Full ATF is on-going for amiga.

powerpc:
- Kernel is just working for all subarchs: oea, booke, ibm4xx (405 and
  strictly-alignment 403).

sh3el:
- Kernel is broken [20]. Seems like regressions for function inlining;
  see also [8] for userland. But, -fno-inline does not work unfortunately...

(rin)

switch gdb to 13.20 for x86_64

(christos)

reorder

(christos)

delete the texinfo parts

(christos)

copy the Makefile from gdb.

(christos)

Make this build

(christos)

regen

(christos)

Don't try to switch to thread on signals generated by the shell.

(christos)

put back libkvm for amd64.

(christos)

- simplify by using PROGDPLIBS
- need --Whole-archive for libgdb to attach modula2, otherwise the file
  does not end up in the list of dependencies from .a archive.

(christos)

lint: since C99, a non-void function must return a value

(rillig)

tests/lint: document how much of C99 lint already implements

(rillig)

xcall(9): Rename condvars to be less confusing.

The `cv' suffix is not helpful and `xclocv' looks like some kind of
clock at first glance.  Just say `xclow' and `xchigh'.

(riastradh)

xen/x86: Get the right intrframe pointer in ddb ipi.

This was broken with the transition from evtchn_set_handler to
intr_establish_xname in 2017, remained broken with the transition
from intr_establish_xname to xen_intr_establish_xname in 2018, and
still remained broken when xen_intr_establish_xname was changed back
to evtchn_set_handler in 2020.

The mechanism is grody -- instead of a secret second argument to the
interrupt handler, the intrframe pointer should be replaced by a
struct cpu_info member that is saved and restored by the interrupt
handler calling logic.  But we should make sure the replacement
actually works first -- which is not trivial in part because the
users are hidden behind sketchy function pointer casts.

With any luck, this will make `mach cpu N' work in ddb on Xen.

XXX pullup-10
XXX pullup-9 (by patch)

(riastradh)

note sparc & sparc64 seem to work fine except for sanitizers.

(mrg)

regen.

(andvar)

fix duplicate definition.

(andvar)

Regen.

(andvar)

Add device ids of the VX800 chipset and s3 chrome 500 series GPU.
Descriptions mainly aligned with VX800/820 Series System Programming Manual.

(andvar)

xen/x86: Enable heartbeat checks.

(riastradh)

tests/crypto/opencrypto: test_asymfeat requires privileges.

(riastradh)

tests/net/inpcb: Tests require root.

(riastradh)

tests/net/net/t_bind: IP_BINDANY and IPV6_BINDANY require root.

(riastradh)

tests/lib/librumphijack: Avoid trying to run rpcbind as non-root.

Can probably make this work through rumphijack, but there's no sense
in even trying the test if we can't, so let's reduce the unprivileged
false alarms.

(riastradh)

tests/lib/libnvmm: Tests require privileges.

(riastradh)

t_nullmnt: Need privileges for mount.

(unless vfs.generic.usermount=1 but let's keep it simple)

(riastradh)

tests/include/t_paths: Test all paths, nonfatally.

This way a single failure doesn't suppress failure reports for all
the other paths to test.

Omit some needless blank lines while here.

(riastradh)

tests/include/t_paths: /dev/ksyms requires root.

(riastradh)

Revert "rump: Set mp_online = true and start threads _after_ cold = 0."

This breaks some tests, e.g. dev/scsipi/t_cd:noisyeject, which relies
on config_finalize to wait for driver threads.  Trouble is, the
actual setting of cold=0 happens near the call to config_finalize in
RUMP__FACTION_DEV.  Need to think harder about this.

(riastradh)

cprng_fast(9): Drop and retake percpu reference across cprng_strong.

cprng_strong may sleep on an adaptive lock (via entropy_extract),
which invalidates percpu(9) references.

Discovered by stumbling upon this panic in a test run:

panic: kernel diagnostic assertion "(cprng == percpu_getref(cprng_fast_percpu)) && (percpu_putref(cprng_fast_percpu), true)" failed: file "/home/riastradh/netbsd/current/src/sys/rump/librump/rumpkern/../../../crypto/cprng_fast/cprng_fast.c", line 117

XXX pullup-10

(riastradh)

cprng(9): Drop and retake percpu reference across entropy_extract.

entropy_extract may sleep on an adaptive lock, which invalidates
percpu(9) references.

Add a note in the comment over entropy_extract about this.

Discovered by stumbling upon this panic during a test run:

[  1.0200050] panic: kernel diagnostic assertion "(cprng == percpu_getref(cprng_fast_percpu)) && (percpu_putref(cprng_fast_percpu), true)" failed: file "/home/riastradh/netbsd/current/src/sys/rump/librump/rumpkern/../../../crypto/cprng_fast/cprng_fast.c", line 117

XXX pullup-10

(riastradh)

lint: implement __builtin_offsetof for the simplest cases

Cases not covered:
1. C99 allows designators in the offsetof macro.
2. For packed types, the offset is likely to be incorrect.

(rillig)

tests/lint: fix test for packed structs on 32-bit platforms

(rillig)

tests/lint: test C99 printf conversion specifiers in lint2

(rillig)

s/acccept/accept/ in comment.

(andvar)

base/md.amd64, base/md.sparc64: Mark openssl compat directories.

Should fix MKCOMPAT=no build.

PR port-amd64/57567

(riastradh)

comp/mi: /usr/include/g++/bit is gcc-only, not for clang (or pcc)

(riastradh)

rump: Set mp_online = true and start threads _after_ cold = 0.

Otherwise we may have threads running while cold, which is a
contradiction in terms.

Deferring mp_online = true is necessary because things like xcall(9)
use rely on it to decide whether to wait for threads on other CPUs.

(riastradh)

memfd(2): Run all tests; don't stop after the first failure.

(riastradh)

revert debug data for libtsan to previous version, too.

XXX Perhaps this should be done by obsoleting the 2.0 file?  For now
XXX this will require manual cleaning of the no-longer-used 2.0 file.

(pgoyette)

t_ubsan, t_ubsanxx: Remove gcc=10, gcc=12 conditionals.

These are built unconditionally.  Should help fix the clang build.

(riastradh)

Tickets #311 and #312

(martin)

Pull up following revision(s) (requested by riastradh in ticket #312):

sys/arch/xen/xen/xennetback_xenbus.c: revision 1.113
sys/arch/xen/xen/xennetback_xenbus.c: revision 1.114
sys/arch/xen/xen/xennetback_xenbus.c: revision 1.115

Revert "xennetback(4): Omit needless membars in xennetback_connect."
PR kern/57560

Revert "xennetback(4): Fix membars in xennetback_rx_copy_process."
PR kern/57560

Revert "xennetback(4): Fix xennetback_evthandler loop."
PR kern/57560

(martin)

Ticket #1709

(martin)

Pull up following revision(s) (requested by manu in ticket #1709):

sys/dev/usb/umodeswitch.c: revision 1.6

Add support for D-Link DWM-222 4G LTS USB adapter

Oddly, the fake umass device does not detach after umodeswitch does
its duty, but functionality is there, thanks to five u3g devices that
attach. u3g devices 0, 3 and 4 does not seem to accept AT commands.
u3g devices 1 and 2 are fine to be used as modems.

(martin)

Pull up following revision(s) (requested by manu in ticket #311):

sys/dev/usb/umodeswitch.c: revision 1.6

Add support for D-Link DWM-222 4G LTS USB adapter

Oddly, the fake umass device does not detach after umodeswitch does
its duty, but functionality is there, thanks to five u3g devices that
attach. u3g devices 0, 3 and 4 does not seem to accept AT commands.
u3g devices 1 and 2 are fine to be used as modems.

(martin)

allow this to build on powerpc*.

(mrg)

Regen.

(msaitoh)

Add Intel I226 devices.

(msaitoh)

Fix some descriptions of Intel Snow Ridge.

(msaitoh)

Revert "xennetback(4): Fix xennetback_evthandler loop."

PR kern/57560

(riastradh)

Revert "xennetback(4): Fix membars in xennetback_rx_copy_process."

PR kern/57560

(riastradh)

Revert "xennetback(4): Omit needless membars in xennetback_connect."

PR kern/57560

(riastradh)

gcc/usr.bin: Sprinkle -fno-jump-tables more for m68k and friends

Now, gcc builds for m68k native.

(rin)

entropy(9): Disable !cold assertion in rump for now.

Evidently rump starts threads before it sets cold = 0, and deferring
the call to rump_thread_allow(NULL) in rump.c rump_init_callback
until after setting cold = 0 doesn't work either -- rump kernels just
hang.  To be investigated -- for now, let's just stop breaking
thousands of tests.

(riastradh)

+RAT  register allocation table

(jschauma)

tyops:
* redicection -> redirection
* escaoed -> escaped

Noted by J. Lewis Muir on netbsd-docs@

(jschauma)

Tickets #1699 - #1708

(martin)

Pull up following revision(s) (requested by jakllsch in ticket #1705):

sys/dev/ic/rtl81x9var.h: revision 1.58
sys/dev/ic/rtl81x9reg.h: revision 1.54
sys/dev/ic/rtl8169.c: revision 1.167
sys/dev/ic/rtl8169.c: revision 1.168

re(4): misc chip revision support changes
* remove impossible-to-match chip revision cases
* bring support for modern chips in line with FreeBSD and OpenBSD
  * adds support for RTL8168GU

Addresses PR kern/56312.

- Print chip revision. From OpenBSD.
- Rename RTK_HWREV_8168_SPIN[123] to RTK_HWREV_8168'B'_SPIN[123].
  Same as other *BSDs.
- Rename RTK_HWREV_8168G_SPIN4 to RTK_HWREV_8411B. Same as other *BSDs.
- Add definition of RTK_HWREV_8169_8110SCE.

(martin)

Tickets #305 - #310

(martin)

Tickets #1878 - #1885

(martin)

Apply patch, requested by ozaki-r in ticket #1885:

sys/net/bpf.c (apply patch)

bpf: allow to read with no filter (regressed at revision 1.213,
fixed differently in -current)

(martin)

Apply patch, requested by ozaki-r in ticket #1708:

sys/net/bpf.c (apply patch)

bpf: allow to read with no filter (regressed at revision 1.213,
fixed differently in -current)

(martin)

README.gcc12: Updated m68000 and m68k

- Kernel works just fine for sun2. Once-observed error was due to
  misc/57562.
- Kernel and bootloader work just fine for amiga.
- Userland needs COPTS.strsuftoll.c+=-fno-stack-protector.
- For amiga, no regression for tests/lib/libc/{sys,gen}.

(rin)

Pull up following revision(s) (requested by ozaki-r in ticket #1884):

sys/netinet6/in6.c: revision 1.289
sys/netinet6/ip6_output.c: revision 1.234

in6: clear ND6_IFF_IFDISABLED to allow DAD again on link-up

in6: don't send any IPv6 packets over a disabled interface

(martin)

Pull up following revision(s) (requested by ozaki-r in ticket #1707):

sys/netinet6/in6.c: revision 1.289
sys/netinet6/ip6_output.c: revision 1.234

in6: clear ND6_IFF_IFDISABLED to allow DAD again on link-up

in6: don't send any IPv6 packets over a disabled interface

(martin)

Pull up following revision(s) (requested by ozaki-r in ticket #310):

sys/netinet6/in6.c: revision 1.289
sys/netinet6/ip6_output.c: revision 1.234

in6: clear ND6_IFF_IFDISABLED to allow DAD again on link-up

in6: don't send any IPv6 packets over a disabled interface

(martin)

Pull up following revision(s) (requested by ozaki-r in ticket #1883):

sys/netinet6/in6_src.c: revision 1.92

in6: add missing rtcache_unref to in6_selectroute

By default, this issue is harmless.  However, if NET_MPSAFE
is enabled, it could eventually lead to a kernel panic.

(martin)

Pull up following revision(s) (requested by ozaki-r in ticket #1706):

sys/netinet6/in6_src.c: revision 1.92

in6: add missing rtcache_unref to in6_selectroute

By default, this issue is harmless.  However, if NET_MPSAFE
is enabled, it could eventually lead to a kernel panic.

(martin)

Pull up following revision(s) (requested by ozaki-r in ticket #309):

sys/netinet6/in6_src.c: revision 1.92

in6: add missing rtcache_unref to in6_selectroute

By default, this issue is harmless.  However, if NET_MPSAFE
is enabled, it could eventually lead to a kernel panic.

(martin)

Pull up following revision(s) (requested by riastradh in ticket #1704):

xsrc/external/mit/MesaLib/dist/src/glx/glxcurrent.c: revision 1.4 (patch)

mesa: Remove massive kludge that worked around PR toolchain/50277.

Now that the underlying bug in ld.elf_so is fixed, the workaround is
causing harm.

(martin)

Pull up following revision(s) (requested by riastradh in ticket #308):

xsrc/external/mit/MesaLib/dist/src/glx/glxcurrent.c: revision 1.4
xsrc/external/mit/MesaLib.old/dist/src/glx/glxcurrent.c: revision 1.2

mesa: Remove massive kludge that worked around PR toolchain/50277.

Now that the underlying bug in ld.elf_so is fixed, the workaround is
causing harm.

(martin)

sc(4) at vme(4): Fix panic due to false ENOMEM for DMA buffer

Similar fix to "sc(4) at mbmem(4)" one; make sure flags are correctly
initialized.

sun3 is not affected.

(rin)

Apply patch, requested by riastradh in ticket #1882 (issue solved differently
in -current):

sys/kern/init_main.c (apply patch)

PR kern/55906: create the aiodone workqueue before running mountroothooks.

(martin)

Pull up following revision(s) (requested by riastradh in ticket #1703):

sys/fs/ptyfs/ptyfs_vnops.c: revision 1.61

PR/55821: tar can not extract base.tgz anymore (./dev/pts and mounted ptyfs)

Allow chown/chmod at the root of ptyfs.

(martin)

Pull up following revision(s) (requested by riastradh in ticket #307):

sys/external/bsd/drm2/dist/drm/i915/gt/intel_ggtt.c: revision 1.16

i915: Fail gracefully, don't panic, with unsupported ggtt views.

Workaround for part of PR kern/56648.

(martin)

Pull up following revision(s) (requested by riastradh in ticket #1881):

usr.sbin/ldpd/socketops.c: revision 1.36
usr.sbin/ldpd/fsm.c: revision 1.16
usr.sbin/ldpd/ldp_peer.c: revision 1.19

ldpd(8): Fix address of misaligned packed members.

PR kern/56895

(martin)

Pull up following revision(s) (requested by riastradh in ticket #1702):

usr.sbin/ldpd/socketops.c: revision 1.36
usr.sbin/ldpd/fsm.c: revision 1.16
usr.sbin/ldpd/ldp_peer.c: revision 1.19

ldpd(8): Fix address of misaligned packed members.

PR kern/56895

(martin)

Add support for D-Link DWM-222 4G LTS USB adapter

Oddly, the fake umass device does not detach after umodeswitch does
its duty, but functionality is there, thanks to five u3g devices that
attach. u3g devices 0, 3 and 4 does not seem to accept AT commands.
u3g devices 1 and 2 are fine to be used as modems.

(manu)