Ticket #1596

(martin)

Pull up following revision(s) (requested by jnemeth in ticket #1596):

sys/dev/pci/mpii.c: revision 1.25

make this compile without bio(4)

(martin)

Tickets #1042 - #1044

(martin)

Pull up following revision(s) (requested by jnemeth in ticket #1044):

sys/dev/pci/mpii.c: revision 1.25

make this compile without bio(4)

(martin)

Pull up following revision(s) (requested by mrg in ticket #1042):

sys/dev/sdmmc/if_bwfm_sdio.c: revision 1.19
sys/dev/sdmmc/ld_sdmmc.c: revision 1.38
sys/dev/sdmmc/sdmmcvar.h: revision 1.35
sys/dev/sdmmc/if_bwfm_sdio.c: revision 1.5
sys/dev/ic/bwfm.c: revision 1.26
sys/dev/ic/bwfm.c: revision 1.27
sys/dev/sdmmc/if_bwfm_sdio.c: revision 1.20
sys/dev/sdmmc/if_bwfm_sdio.c: revision 1.21
sys/dev/sdmmc/sdmmc_io.c: revision 1.20
sys/dev/sdmmc/sdmmc_mem.c: revision 1.72
sys/dev/sdmmc/sdmmc.c: revision 1.40
sys/dev/sdmmc/sdmmc_ioreg.h: revision 1.6
sys/dev/sdmmc/if_bwfm_sdio.c: revision 1.16

Don't pass empty mbufs to the network stack.

Avoid changing signedness bit with << in sdmmc_ioreg.h
Reported by <prlw1>

If the controller doesn't support switch func (opcode 6) then skip
setting this but continue with other settings.  This allows us to use
a card, albeit at a lower speed.

Fix races in sdmmc tasks and teach ld@sdmmc to abort xfers on detach.
- Teach sdmmc_add_task to queue it only if not already queued.
- Remove now-redundant logic to avoid repeated queueing elsewhere.
- Teach sdmmc_del_task to wait until task has completed.
- Call sdmmc_del_task in various needful places.
- Replace abuse of pcq by a lock and a tailq.
  (pcq is multi-producer, _single_-consumer, but there are potentially
  multiple consumers here and really only one producer.)
- Teach ld_sdmmc to abort xfers on detach.
  (Mechanism is kinda kludgey but it'll do for now; any effort one is
  tempted to spend overhauling this should be spent overhauling sdmmc
  to support proper asynchronous commands.)
- Make sure ld_sdmmc_discard either returns failure or eventually calls
  ldenddiscard.

XXX Currently ld_sdmmc_detach aborts xfers _before_ ldbegindetach has
has committed to detaching or not.  This is currently necessary to
avoid a deadlock because ldbegindetach waits for xfers to drain --
which strikes me as wrong; ldbegindetach shouldn't wait for anything,
and should only make the decision to commit to detaching or not so
the caller can decide whether to abort xfers before we actually wait
for them in ldenddetach.

XXX pullup -- although this changes some kernel symbols (sdmmc_add_task
and sdmmc_del_task), it shouldn't affect any existing modules; the only
module that uses sdmmc is ld_sdmmc.kmod, which is `.if 0' in the build
so there shouldn't be any of them floating around.

Make this work on big endian machines

move some of the patching of callbacks and other data after
ieee80211_ifattach() but before if_deferred_start_init().
may fix panic i saw in after restarting wpa_supplicant.
from mlelstv.

only ask for SDPCMD_INTSTATUS_HMB_SW_MASK and SDPCMD_INTSTATUS_CHIPACTIVE
interrupts, not all of them.  we only ack these ones.
mostly fixes pinebookpro wifi hard hangs.  still is problematic and can
trigger interrupt storm that appears as a hard hang without NET_MPSAFE,
and a follow up, less clearly right, change will reduce that to a soft
hang of the interface that can be cleared with 'ifconfig bwfm0 down up',
and even often recovers itself now.

clear all interrupts, not just those we expect from the hostintmask.
this removes the final hard hang i have seen in pinebookpro wifi,
though one may still need to 'ifconfig bwfm0 down up' occasionally,
so we still have bugs to fix here (the hang is usually associated
with 'checksum error' from bwfm/sdio.)

Sort #includes.  Nix trailing whitespace.
No functional change intended.

(martin)

make(1): revert C99 initializer in ApplyModifiers

The code of usr.bin/make is supposed to be C90-compatible.  That's why
it neither uses line-end comments nor declaration-after-statement nor a
few other features.

The fields that were copied "by name" did not get any additional
comments, only the ones with literal values did, since it's hard to see
what these mean.

This style of initializer has the additional benefit that a missing or
extraneous initializer-item would lead to a compile-time error, rather
than going undetected.

(rillig)

Add TOFU

(christos)

make(1): mark inconsistent word separators for variable modifiers

(rillig)

make(1): improve type signature of Var_Export

(rillig)

make(1): add test for non-obvious .MAKE.EXPORTED edge case

(rillig)

Put probed framebuffer info to a log file by default.

(tsutsui)

make(1): extend the documentation for variable flags

(rillig)

make(1): format code in str.c consistently

(rillig)

make(1): clean up indentation, includes, add documentation

(rillig)

make(1): document a hard-to-understand pointer calculation

(rillig)

make(1): add more tests for Cmd_Exec

(rillig)

make(1): remove outdated comment

(rillig)

make(1): avoid undefined behavior in Cmd_Exec

Iterating the command output backwards was dangerous since at the end,
the pointer cp pointed outside of the array.  Even without dereferencing
this pointer, this already invokes undefined behavior (C11, 6.5.6p8).
Don't risk anything.  Iterating forwards is probably faster anyway, since
it is more common.

(rillig)

ONe '#' is enough for a comment

(skrll)

fix a couple of minor issues:
- un_ed is not a function, but an array
- fix a typo
- add a blank line after a list

(mrg)

make(1): add test for null byte in the output of a command

(rillig)

Fix another UVMHIST so it doesn't use %s

(skrll)

make(1): remove redundant assignment from Cmd_Exec

A Buffer is always null-terminated.

(rillig)

make(1): split local variable in Cmd_Exec into two

This avoids a mismatch between signed and unsigned types.

(rillig)

More whitespace

(skrll)

defflag foo on each line to make searching easier.

sort some lines and fix some indentation while I'm here.

(skrll)

This file is only ever used when MULTIPROCESSOR so unifdef MULTIPROCESSOR

(skrll)

Use compiler defines to determine which LLSCSYNC, et al
to provide.

This should fix mips builds.

(skrll)

make(1): add test that demonstrates possible delimiters for :S

(rillig)

make(1): explain the mod-subst-dollar test

(rillig)

Remove redundant command option arg checks.

(tsutsui)

Remove a leftover variable for non-XKB autorepeat.

(tsutsui)

Don't use %s in UVMHIST_PRINT.  Remove an unnecessary #ifdef UVMHIST while
I'm here

(skrll)

make(1): add another test case for mod-subst-dollar

Having only 8 dollar signs does not prove anything.  It might still be
the result of 3 substitutions in a row.  Having 5 substitutions in a row
is less likely though.

(rillig)

make(1): restrict the type of startc and endc to char

(rillig)

Add a comment

(skrll)

Type consistency

(skrll)

make(1): use fixed-size arrays for Enum_ToString

Declaring the ToStringSize as "static const size_t" made it an ordinary
integer expression.  To avoid variable length arrays, the commonly
accepted way is to declare the length as an enum constant, as that is
considered an integer constant expression, which in turn makes the
declaration a fixed-size array.

(rillig)

KNF

(skrll)

Inform detected keyboard type and layout via LogMessage().

(tsutsui)

Don't kcpuset_clone every pmap_tlb_shootdown_bystanders.  Instead allocate
a kcpuset_t per cpu_info and use that.

(skrll)

make(1): allow to build using GCC 9 during development

(rillig)

Fix build; gcc does not like VLA's, so hard code the boundary
Use c99 initializers

(christos)

Fix some clang neon intrinsics.

Compile-tested only, with -Wno-nonportable-vector-initializers.  Need
to address -- and test -- this stuff properly but this is progress.

(riastradh)

Use vshlq_n_s32 rather than vsliq_n_s32 with zero destination.

Not sure why I reached for vsliq_n_s32 at first -- probably so I
wouldn't have to deal with a new intrinsic in arm_neon.h!

(riastradh)

Nix outdated comment.

I implemented this parallelism a couple weeks ago.

(riastradh)

Fix mistake in big-endian arm clang.

Swapped the two halves (only gcc does that, I think) and wrote j,i
backwards, oops.

(I don't have a big-endian arm clang build handy to test; hoping this
works.)

(riastradh)

Add missed bpf(4) node for dhcpcd(8) in INSTALL floppies.

Should be pulled up to netbsd-9.

(tsutsui)

Use the right size for several calloc calls.

When allocating for a Char **, it should use sizeof(Char *), not
sizeof(Char **). This doesn't actually affect the results except
on DS9000 though :-)

(part 2, the instance in this file was as far as I can tell
inexplicably missed by CVS on the first go...)

(dholland)

Clarify some comments.

(dholland)

Use the right size for several calloc calls.

When allocating for a Char **, it should use sizeof(Char *), not
sizeof(Char **). This doesn't actually affect the results except
on DS9000 though :-)

(dholland)

Don't cast the value returned from *malloc. No change to compiler output.

(dholland)

add commented out entries for onewire at snapper, and document what they're for

(macallan)

add support for the onewire bus found in some macs, namely Quicksilver.
This can be used to read the EEPROM content from Apple Pro speakers, or to
hook up other onewire devices.

(macallan)

make this compile without bio(4)

(jnemeth)

regen for a.out vectors

(christos)

regen for a.out vectors

(christos)

Put back the a.out netbsd and bsd vector. They are useful for debugging
old a.out binaries and take ~0 space.

(christos)

make(1): merge duplicate code for the :H :T :R :E modifiers

By setting modifyWord first, the rest of the code becomes exactly the
same and is merged by the compiler.

(rillig)

PR/55547: Dan Plassche: Fix BSD/OS binary emulation.
Centralize lcall sniffer and recognize the BSD/OS flavor.

(christos)

Fix the OTIOCGETD emulation. Line discipline 0 is NTTYDISC.

(christos)

make(1): remove trailing Z from buffer functions

This Z had been useful during the migration from int to size_t.  This
migration is finished, at least for the Buffer type, so the Z is no
longer necessary.

(rillig)

make(1): add debug logging for Var_Parse

This will hopefully help with tracking down why the "Undefined variable"
error message is not triggered.

There is some other non-obvious behavior nearby.  In Parse_DoVar, the !=
assignment operator evaluates the variable using VARE_UNDEFERR, but
there is not even a warning for the following line:

!= echo err ${UNDEFINED} 1>&2

(rillig)

make(1): mark condition strings as constant

(rillig)

make(1): remove redundant documentation from cond.c

Many of the functions in cond.c are so small that it's faster to read
their code instead of a large block of documentation.

There are other functions that actually need a detailed description.
These have been left as-is.

(rillig)

make(1): remove redundant function prototypes from cond.c

(rillig)

PR/55551 Soumendra Ganguly: Simplify tcgetattr error handling.

(christos)

make(1): fix typo in test

(rillig)

Fix ARM NEON implementations of AES and ChaCha on big-endian ARM.

New macros such as VQ_N_U32(a,b,c,d) for NEON vector initializers.
Needed because GCC and Clang disagree on the ordering of lanes,
depending on whether it's 64-bit big-endian, 32-bit big-endian, or
little-endian -- and, bizarrely, both of them disagree with the
architectural numbering of lanes.

Experimented with using

static const uint8_t x8[16] = {...};

        uint8x16_t x = vld1q_u8(x8);

which doesn't require knowing anything about the ordering of lanes,
but this generates considerably worse code and apparently confuses
GCC into not recognizing the constant value of x8.

Fix some clang mistakes while here too.

(riastradh)

make(1): fix CRLF line endings in newly added files

(rillig)

make(1): extend debug logging to error values

The error marker var_Error is just an empty string.  In the debug log
this empty string was not distinguishable from an otherwise empty
string.

Having this distinction helps in understanding the exact data flow.

(rillig)

make(1): add more detailed debug logging for variable modifiers

Before a modifier is applied to a variable, it is not yet parsed,
therefore it is only possible to log a rough estimate of the modifier.
But after applying it, the parsing position has advanced, and the full
modifier can be logged.

In addition, to fully understand how the modifiers work, it's not enough
to just know the variable names and values, there are also some flags
that influence how the modifiers behave.  The most influential is
VARE_WANTRES.

Thanks to sjg for the extensive review and valuable feedback on the
first drafts.

(rillig)

make(1): improve documentation of Var_Parse and reorder conditions

(rillig)

make(1): fixup for "Unfinished modifier"

(rillig)

make(1): improve error message in case of unfinished modifiers

The previous error message "Unclosed substitution" was wrong for several
reasons.

It is not about "unclosed", but about "unfinished" since in the
:@var@...@ modifier the missing '@' does not really close anything.

The word "substitution" may have originated in a time where :S and
:from=to were the only modifiers, and these were indeed substitutions,
but several other modifiers aren't.

The :S and :C modifiers allow an arbitrary delimiter, therefore it is
helpful to enclose the delimiter in quotes, just in case someone chooses
')' or '{' or even ' ' as delimiter.

(rillig)

make(1): align the code in Var_Append with Var_Set

The code has the same effect in both functions, therefore it should also
look the same.

(rillig)

make(1): consistently use postfix-increment

(rillig)

make(1): add test for the :gmtime modifier with indirect time

(rillig)

make(1): clean up VarStrftime

The parameter names were confusing and had outdated types.

(rillig)

make(1): add test for unknown sub-modifier of the :S modifier

(rillig)

make(1): clean up Var_UnExport

Mark the parameter as constant since it is not modified.

Remove tests for '\n' since these can never succeed.

newenv can never be NULL since neither of bmake_malloc or bmake_realloc
returns NULL.

Improve variable names: vlist was too unexpressive.

Add debug logging since unexporting variables is an uncommon operation
that directly affects the observable environment of the child processes.

Fix CRLF line endings in a few unit tests.

(rillig)

make(1): clean up Var_Export

The string from the .export directive can never be NULL.

The test for local single-char variables is already done in Var_Export1.

(rillig)

make(1): change return type of Var_Export1 to Boolean

(rillig)

make(1): fix yoda-style comparisons in var.c

(rillig)

make(1): condense comment for ApplyModifiers

This comment only repeats what is written in the manual page.
Furthermore, it didn't get updated consistently.  The missing modifiers
were :_, :gmtime, :localtime, :hash, :Q, :range, :Or.

(rillig)

make(1): fix debug output for indirect modifiers

The trailing part after the modifier was confusing at best.  It does
make sense to log the string from p to p+rlen, but not from p+len to
p+len+len.

Consistently use double quotes for strings.

(rillig)

make(1): add test for debugging message for indirect modifiers

The current output format stops in the middle of the next modifier,
which was probably not intended.

(rillig)

Find the if a device points to an active filesystem by looking at the mount
list.

(christos)

the drawing engine needs a stride that's a multiple of 8 in pixels, so
let's actually distinguish between width and stride, and always round the stride
up to the next multiple of 8
now modes with odd widths work

(macallan)

make(1): format the code in var.c a little more consistently

(rillig)

Remove trailing whitespace.

(wiz)

make(1): add tests for creative variable names in the :@ modifier

(rillig)

make(1): add test for exporting variables

(rillig)

pcu_available_p is only used in KASSERT(), fix non-diagnostic build.

(christos)

Also set the bits for horizontal sync start delay.  This makes machfb work
correctly for some modes (e.g. 1152x720).
Modify mach64_get_mode() to get the mode from the chip registers (only used
with debug on).
Whilst here tidy up some other debug output.

(jdc)

accmode should be accmode_t

(christos)

Catch up with genfs_can argument changes

(christos)

Catch up with lktype addition.

(christos)

make(1): document why the suffixes test must stay disabled

(rillig)

make(1): enable test phony-end

This at least documents the actual behavior.  Not sure what the expected
behavior is and why.

(rillig)

Use CPU_IS_PRIMARY macro on alpha and sparc64.

(fcambus)

make(1): enable test for .IMPSRC

Having this test disabled was very confusing since its content didn't
match the actual behavior, and this also differs from the GNU make
behavior.

(rillig)

PR/55548: Soumendra Ganguly: Since isatty(3) is implemented using
tcgetattr(3), call it directly to avoid calling it twice. This
makes error handling more precise. Also don't call err(3) when
tcsetattr(3) fails.

(christos)

Provide a pmap_segtab_deactivate for symmetry with pmap_segtab_activate
and use it in pmap_deactivate

Call pmap_md_xtab_{,de}activate from pmap_segtab_{,de}activate to be used
for PMAP_HWPAGEWALKER and any caches ops that might be required.

Provide empty (for now) pmap_md_xtab_{,de}activate functions on the
platforms that use sys/uvm/pmap

(skrll)

make(1): one file per line in the Makefile

Suggested by sjg.

(rillig)

s/developement/development/

(snj)

fix typo.
new sentence, new line.

(snj)

make(1): use consistent name for result of Cmd_Exec

(rillig)

make(1): reduce code size in :D and :U modifier

This affects both the source code size and the binary code size, at
least on x86_64.

(rillig)

make(1): clean up code for variable handling

The VarFlags type doesn't need an underscore.  The underscore is
typically only used for exported functions.

Document the memory allocation details for Var.name.

Use consistent names for Hash_Entry variables.  Quite possibly one of
them was a Lst_Node in ancient times, but that's not a reason to keep
this variable name forever.

(rillig)

make(1): remove unused macro Hash_Size

(rillig)

Use -r for recursive

(sjg)

Update test result

(sjg)

Remove VARE_WANTRES for LINT

We need the parsing checked.
I might make sense to add a VARE_LINT flag for corner cases.
Time will tell.

Reviewed by: rillig

(sjg)

Centralise SYNC/BDSYNC in asm.h and introduce a new LLCSCSYNC and use it
before any ll/sc sequences.

Define LLSCSYNC as syncw; syncw for cnMIPS - issue two as early cnMIPS
has errat{um,a} that means the first can fail.

(skrll)

add missing {IP,IP6}_STAT_NOIPSEC to netstat.

(knakahara)

No need to recover from fault from within a hardware interrupt handler.

(ryo)

revert the changes of http://mail-index.netbsd.org/source-changes/2020/08/03/msg120183.html

This change is overengineered.
bus_space_{peek,poke}_N does not have to be reentrant nor available for interrupt context.

requested by skrll@

(ryo)

make(1): add rationale and expected behavior to "recursive" test

(rillig)

make(1): add test for unintended "recursive variable" in -dL mode

(rillig)

make(1): revert previous commit; "make retest" was already possible

What I really meant to allow was to run "make sync-mi" directly from the
main directory.  But adding that to TARGETS didn't do anything.

(rillig)

make(1): allow "make retest" directly from the main directory

(rillig)

Accidently not commited for ticket #1595:

sys/arch/x86/include/specialreg.h              1.129 via patch

Add six errata for AMD Family 17h (Ryzen etc).

(martin)

Tickets #1584 - #1595

(martin)

Pull up the following, requested by msaitoh in ticket #1595:

sys/arch/x86/include/specialreg.h 1.129 via patch
sys/arch/x86/x86/errata.c 1.24-1.26

- Add six errata for AMD Family 17h (Ryzen etc), tested by
  Patrick Welche and mrg@.

(martin)

Pull up the following revisions, requested by msaitoh in ticket #1594:

sys/dev/pci/if_wm.c 1.655-1.658, 1.660,
1.662, 1.664-1.668,
1.671-1.674, 1.678,
1.680-1.685 via patch
sys/dev/pci/if_wmreg.c 1.118-1.119 via patch
sys/dev/pci/if_wmvar.c 1.45 via patch
sys/dev/mii/igphy.c 1.35-1.36 via patch
sys/dev/mii/igphyreg.h 1.12-1.13
sys/dev/mii/makphy.c 1.66 via patch
sys/dev/mii/makphyreg.h 1.11

- Add SFP support. Module insertion/removal is not supported yet.
  Currently, SFP detection is only done in the driver's attach phase.
- Detect the Media Auto Sense feature. Not supported yet.
- Fix SFF_SFP_ETH_FLAGS_100FX. It's not 0x10 but 0x20.
- Add extra delay in wm_serdes_power_up_link_82575().
- Add Intel I219 LM10-LM15 and V10-V14.
- wm(4) can use workqueue as deferred Rx/Tx handler).
  Set hw.wm*.txrx_workqueue=1 to use workqueue instead of softint.
  The default value of hw.wm*.txrx_workqueue is 0 which use softint
  as before.
- Unset RSS UDP flags like ixg(4) and other OSes. To handle IP
  fragmented UDP, first packet and second packet should be processed
  in the same Rx queue.
- It's useless to not to set PCI_PMCSR_PME_STS bit when writing because
  the bit is W1C. Instead, always write PCI_PMCSR_PME_STS bit to clear
  in case it's already set.
- Actually writing always the checksum offload context descriptor
  makes the HW do extra processing, avoid doing that if possible.
- Fix a bug that the WMREG_EEARBC_I210 register is incorrectly set if
  the system uses iNVM.
- "wmX: 0" on 82542 is difficult to understand, so don't print it.
- Explicitly cast from uint16_t to uint32_t before shifting 16bit left
  when printing Image Unique ID to avoid undefined behavior.
- Set if_baudrate for non-MII device.
- Rename some macros and function.
- KNF. Add comment.

(martin)

Add CTASSERT.

(maxv)

Pull up the following revisions, requested by msaitoh in ticket #1593:

sys/arch/x86/conf/files.x86 1.108
sys/arch/x86/include/apicvar.h 1.7 via patch
sys/arch/x86/include/cpu.h 1.121
sys/arch/x86/x86/cpu.c 1.185 via patch
sys/arch/x86/x86/hyperv.c 1.7
sys/arch/x86/x86/tsc.c 1.41
sys/arch/xen/conf/files.xen 1.181

Get TSC frequency from CPUID 0x15 and/or x16 if it's available.
This change fixes a problem that newer Intel processors' timer
counts very slowly.

(martin)

Pull up following revision(s) (requested by msaitoh in ticket #1592):

sys/dev/sdmmc/sdhc.c: revision 1.107
sys/dev/sdmmc/sdhcreg.h: revision 1.21

Identify SDHC 4.1 and 4.2. From {DragonFly,Free}BSD.

(martin)

Pull up the following revisions, requested by msaitoh in ticket #1591:

sys/dev/pci/piixpm.c 1.57-1.59,
1.61-1.63 via patch
sys/dev/pci/piixpmreg.h 1.9-1.12

- Fix number of port for Hudson rev. 0x1f and newer.
- Read SB800_SMB_HOSTC correctly. This register is not in the PCI
  config space but in the I/O space.
- The bit 0 of SB800_SMB_HOSTC is 0 on SMI or 1 on IRQ, so invert the
  check.
- Don't force using SMBUS0SEL register.
- Acquire/release host semaphore to share SMBus between the host and
  the embedded controller (IMC). Without this change, "shutdown -r"
  does power off and not boot on some machines.
- Save/restore port number before selecting port.
- Modify comment.
- Whitespace fix.

(martin)

Pull up the following revisions, requested by msaitoh in ticket #1590:

sys/dev/pci/if_ti.c 1.103, 1.106, 1.108,
1.116-1.120 via patch
sys/dev/pci/if_tireg.h 1.26

- Use pci_intr_establish_xname()
- Don't clear CFI and priority bit to pass them to the upper layer.
- Add support for Farallon PN9000SX from FreeBSD.
- u_int_{8,16,32}_t -> uint_{8,16,32}_t
- Fix typo in comment.
- Style fix.

(martin)

Pull up following revision(s) (requested by msaitoh in ticket #1589):

sys/arch/x86/x86/coretemp.c: revision 1.37

  Add special handling for model 0x0f stepping >=2 or mode 0x0e to get Tjmax.

(martin)

Pull up the following revisions, requested by msaitoh in ticket #1588:

sys/arch/x86/include/specialreg.h 1.162-1.168 via patch

- AMD CPUID Fn8000_000a %edx bit 20 is "SPEC_CTRL".
- Add some bit definitions of AMD's CPUID Fn8000_001f Encrypted Memory
  features.
- Add AMD INVLPGB/TLBSYNC hypervisor enable in VMCB and TLBSYNC
  intercept bit.
- Add AMD MSR_DE_CFG's bit 1 as DE_CFG_LFENCE_SERIALIZE.
- Add some definitions for Intel:
  - Add CPUID leaf 6 %eax bit 19 for HW_FEEDBACK* and
    IA32_PACKAGE_TERM* MSRs.
  - Add CPUID leaf 7 %ecx bit 31 for Protection Keys.
  - Add definition of Load only TLB and Store only TLB.
  - Add IF_PSCHANGE_MC_NO bit of IA32_ARCH_CAPABILITIES
  - Fix HWP_IGNIDL.
- Add CPUID 7 %edx bit 9 "SRBDS_CTRL"
- Modify comment. Style and fix typo.

(martin)

Pull up the following revisions, requested by msaitoh in ticket #1587:

sys/dev/pci/ixgbe/ix_txrx.c 1.62-1.63 via patch
sys/dev/pci/ixgbe/ixgbe.c 1.225, 1.228-1.229,
1.232 via patch
sys/dev/pci/ixgbe/ixgbe.h 1.64, 1.66
sys/dev/pci/ixgbe/ixv.c 1.146, 1.148-1.150
via patch
sys/dev/pci/ixgbe/ixgbe_common.c 1.27
sys/dev/pci/ixgbe/ixgbe_vf.c 1.23
sys/dev/pci/ixgbe/ixgbe_82598.c 1.15
sys/dev/pci/ixgbe/ixgbe_x550.c 1.18
sys/dev/pci/ixgbe/ixgbe_netbsd.c 1.14
sys/dev/pci/ixgbe/ixgbe_phy.c 1.21
sys/dev/pci/ixgbe/ixgbe_osdep.h 1.26

- Fix IXGBE_LE32_TO_CPUS() macro for big endian machine. This problem
  was only on X550.
- Add debug printf()s.
- Use unsigned to avoid undefined behavior in
  ixgbe_fc_enable_generic().
- Modify a little to reduce diff between ixgbe.c and ixv.c.
  No functional change.
- Modify comment.
- Remove unused macros.
- Whitespace fix.
- Fix typos.

(martin)

Pull up the following revisions, requested by msaitoh in ticket #1586:

sys/dev/pci/ichsmb.c 1.66-1.68 via patch

- Add Comet Lake, Whiskey Lake U and Amber Lake Y support.
- Whitespace fix.

(martin)

Pull up the following revisions, requested by msaitoh in ticket #1585:

usr.sbin/cpuctl/Makefile 1.9
usr.sbin/cpuctl/arch/cpuctl_i386.h 1.5
usr.sbin/cpuctl/arch/i386.c 1.111-1.113 via patch
usr.sbin/cpuctl/cpuctl.c 1.31
usr.sbin/cpuctl/cpuctl.h 1.7
sys/arch/x86/x86/identcpu_subr.c 1.1-1.7

- Get TSC frequency from CPUID 0x15 and/or x16 for newer Intel
  processors.
- Add 0xa5 and 0xa6 for Comet Lake.
- Rename ci_cpuid_level to ci_max_cpuid and ci_cpuid_extlevel to
  ci_max_ext_cpuid to match x86/include/cpu.h. No functional change.
- Sort some entries.
- Add comment.

(martin)

No need to build fbcmap_mi.c in each DDX server.

Per upstream commit:
https://cgit.freedesktop.org/xorg/xserver/commit/?id=432fc37e2ca833f1ec3cb614cbdc3a7ae13f22b7
> Build fbcmap_mi.c once, rather than once for each DDX, and make it part of libfb
> or libwfb convenience library.

Tested on sun3 and x68k.

(tsutsui)

Add new fields here and there.

(maxv)

Improve the CPUID emulation:

- Hide SGX*, PKU, WAITPKG, and SKINIT, because they are not supported.
- Hide HLE and RTM, part of TSX. Because TSX is just too buggy and we
  cannot guarantee that it remains enabled in the guest (if for example
  the host disables TSX while the guest is running). Nobody wants this
  crap anyway, so bye-bye.
- Advertise FSREP_MOV, because no reason to hide it.

(maxv)

Add new field definitions, and intercept everything, for future-proofness.

(maxv)

Tickets #1036 - #1041

(martin)

Add new field definitions.

(maxv)

Pull up following revision(s) (requested by maxv in ticket #1041):

sys/dev/nvmm/x86/nvmm_x86_vmx.c: revision 1.66
sys/dev/nvmm/x86/nvmm_x86_vmx.c: revision 1.50
sys/dev/nvmm/x86/nvmm_x86_svm.c: revision 1.66
sys/dev/nvmm/x86/nvmm_x86_vmx.c: revision 1.46
sys/dev/nvmm/x86/nvmm_x86_vmx.c: revision 1.49
sys/dev/nvmm/x86/nvmm_x86_svm.c: revision 1.55
sys/dev/nvmm/x86/nvmm_x86_svm.c: revision 1.56

pg->phys_addr > VM_PAGE_TO_PHYS(pg)

Explicitly cast pointers to uintptr_t before casting to enums. They are
not necessarily the same size. Don't cast pointers to bool, check for
NULL instead.

vmx_vmptrst(): only used when DIAGNOSTIC

Simplify, remove unnecessary #ifdef DIAGNOSTIC around KASSERTs.

Use ULL, to make it clear we are unsigned.

(martin)

Make it easier to understand what's going on, no functional change.

(maxv)

Pull up following revision(s) (requested by msaitoh in ticket #1040):

sys/dev/mii/igphy.c: revision 1.35
sys/dev/mii/igphy.c: revision 1.36
sys/dev/mii/igphyreg.h: revision 1.12
sys/dev/mii/igphyreg.h: revision 1.13
sys/dev/mii/makphyreg.h: revision 1.11
sys/dev/pci/if_wm.c: revision 1.682
sys/dev/pci/if_wm.c: revision 1.683
sys/dev/pci/if_wm.c: revision 1.684
sys/dev/pci/if_wm.c: revision 1.685
sys/dev/mii/makphy.c: revision 1.66

s/MII_IGPHY_/IGPHY_/. No functional change.

Rename PSSR_* to MAKPHY_PSSR_* and IGPHY_PSSR_* to avoid conflict.
No functional change.

  Setup PCS and SGMII for SFP correctly. It still doesn't support SFP
insertion/removal.

Copper:
wm2: SGMII(SFP)
wm2: 0x1043c440<SPI,IOH_VALID,PCIE,SGMII,NEWQUEUE,ASF_FIRM,EEE,SFP>
makphy0 at wm2 phy 6: Marvell 88E1111 Gigabit PHY, rev. 1

Fiber:
wm3: SERDES(SFP)
wm3: 0x10034440<SPI,IOH_VALID,PCIE,NEWQUEUE,ASF_FIRM,SFP>
wm3: 1000baseSX, 1000baseSX-FDX, auto

  Explicitly cast from uint16_t to uint32_t before shifting 16bit left
when printing Image Unique ID. Found by kUBSan.

  Set if_baudrate for non-MII device. Before this commit, it was 0.

(martin)

Pull up following revision(s) (requested by skrll in ticket #1039):

sys/arch/hppa/dev/cpu.c: revision 1.2
sys/arch/hppa/hppa/fpu.c: revision 1.27

Don't KASSERT there's an FPU present.  QEMU doesn't have one...

(martin)

Pull up following revision(s) (requested by jmcneill in ticket #1038):

sys/dev/pci/if_ena.c: revision 1.25

PR port-arm/55532: kernel panic with ena on AWS a1.2xlarge

Do not mark callout and workqueues as mpsafe unless the NET_MPSAFE option
is present.

(martin)

Pull up following revision(s) (requested by uwe in ticket #1584):

sys/dev/dev_verbose.h: revision 1.3

DEV_VERBOSE_MODULE_DEFINE - use MODULE_CLASS_DRIVER.

This makes built-in verbose modules available before the start of the
autoconfiguration, when they are needed.  From pgoyette@

PR kern/55535

(martin)

Pull up following revision(s) (requested by uwe in ticket #1037):

sys/dev/dev_verbose.h: revision 1.3

DEV_VERBOSE_MODULE_DEFINE - use MODULE_CLASS_DRIVER.

This makes built-in verbose modules available before the start of the
autoconfiguration, when they are needed.  From pgoyette@

PR kern/55535

(martin)

Pull up following revision(s) (requested by nia in ticket #1036):

distrib/notes/evbarm/hardware: revision 1.22
distrib/notes/evbarm/xfer: revision 1.5
distrib/notes/evbarm/hardware: revision 1.17
distrib/notes/common/main: revision 1.563

Note support for TI AM335x SoC
List all supported Amlogic SoCs
Remove duplicate word
Remove Arm OABI -> EABI change notice

(martin)

Ammend ticket #1582

(martin)