-
Notifications
You must be signed in to change notification settings - Fork 58
New issue
Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.
By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.
Already on GitHub? Sign in to your account
Merge FreeBSD 2024-05-17 #2208
Merge FreeBSD 2024-05-17 #2208
Commits on May 11, 2024
-
nvmecontrol: Appease a meaningless signed error warning thing
Consistently use the weird ssize_t type for things I know are unsigned, but which none-the-less need to be compared to signed things to prevent a bogus warning. Sigh, these aren't bugs, can't possibly be bugs and a waste of time to fix. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 3d966ae - Browse repository at this point
Copy the full SHA 3d966aeView commit details -
/bin/rmdir: Exit with status 2 for invalid arguments
PR: 277677 Signed-off-by: Henrich Hartzer <[email protected]> Reviewed by: imp Pull Request: freebsd/freebsd-src#1161
Configuration menu - View commit details
-
Copy full SHA for 9bcc1b1 - Browse repository at this point
Copy the full SHA 9bcc1b1View commit details -
In some cases, the USB_QUIRK_VP macro was being misused. Instead of setting quirks to the intended value, the first two supplied quirks would go into lo_rev and hi_rev. Replace it with USB_QUIRK_VO which only takes the needed args. This also makes the Dummy products, which where being used to correctly set vendor only quirks, not necessary. Reviewed by: imp Pull Request: freebsd/freebsd-src#1153
Configuration menu - View commit details
-
Copy full SHA for 64e05e9 - Browse repository at this point
Copy the full SHA 64e05e9View commit details -
usb: Remove uneeded revision verbosity from quirks list
Seperate usb quirks that target specific revisions from those that dont. Alot of the quirks dont use lo_rev and hi_rev, so we can abstract the 0x0000, 0xffff into a macro. [[ This commit is a bit more churn than we like. I carefully reviewed each one and they are all good. The end product is better -- imp ]] Reviewed by: imp Pull Request: freebsd/freebsd-src#1153
Configuration menu - View commit details
-
Copy full SHA for 881ae76 - Browse repository at this point
Copy the full SHA 881ae76View commit details -
linprocfs: Add support for proc/sysvipc/{msg,sem,shm}
Signed-off-by: Ricardo Branco <[email protected]> Reviewed by: imp Pull Request: freebsd/freebsd-src#1218
Configuration menu - View commit details
-
Copy full SHA for 099a81a - Browse repository at this point
Copy the full SHA 099a81aView commit details -
linux: Make module standalone-buildable
Add opt_inet.h and opt_usb.h to make linux module buildable standalone. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for c5f906d - Browse repository at this point
Copy the full SHA c5f906dView commit details
Commits on May 12, 2024
-
Cast the time type to (long). This is correct on all architectures. On i386, this promotes the int time_t to a long (which is also 32-bit). On 64-bit architectures, this promotes the 64-bit signed time_t to a 64-bit signed int type. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 02f481a - Browse repository at this point
Copy the full SHA 02f481aView commit details -
cdev_pager_allocate(): ensure that the cdev_pager_ops ctr is called o…
…nly once per allocated vm_object. Otherwise, since constructors are not idempotent, we e.g. leak device reference in case of non-managed pager. PR: 278826 Reported by: Austin Zhang <[email protected]> Reviewed by: alc, markj Tested by: pho Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45113
Configuration menu - View commit details
-
Copy full SHA for e934040 - Browse repository at this point
Copy the full SHA e934040View commit details -
Sponsored by: The FreeBSD Foundation MFC after: 1 week
Configuration menu - View commit details
-
Copy full SHA for 6d79564 - Browse repository at this point
Copy the full SHA 6d79564View commit details -
linprocfs: Really fix time_t type issue
The cast to (long) is wrong on all the other 32-bit platforms. (long long) is the correct type on all platforms. Also, use a z modifier for size_t which also fails on 32-bit platforms. Fixes: 02f481a Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for ee2e366 - Browse repository at this point
Copy the full SHA ee2e366View commit details -
ipfw: Fix a typo in a source code comment
- s/defaul/default/ MFC after: 3 days
Configuration menu - View commit details
-
Copy full SHA for 78e4dbc - Browse repository at this point
Copy the full SHA 78e4dbcView commit details -
Configuration menu - View commit details
-
Copy full SHA for 71ffda4 - Browse repository at this point
Copy the full SHA 71ffda4View commit details -
bsdinstall: Remove unused variables in fetchmissingdists
ALL_DISTRIBUTIONS and VERIFY_MANIFEST_SIG They are neither used in the script nor exported. Not referenced anywhere in bsdinstall/* Approved by: imp@ Differential Revision: https://reviews.freebsd.org/D42369
Configuration menu - View commit details
-
Copy full SHA for 47535ba - Browse repository at this point
Copy the full SHA 47535baView commit details -
arm64: map kernel using large pages when page size is 16K
When the page size is 16K, use ATTR_CONTIGUOUS to map the kernel code and data sections using 2M pages. Previously, they were mapped using 16K pages. Reviewed by: markj Tested by: markj Differential Revision: https://reviews.freebsd.org/D45162
Configuration menu - View commit details
-
Copy full SHA for 94b09d3 - Browse repository at this point
Copy the full SHA 94b09d3View commit details
Commits on May 13, 2024
-
Import _FORTIFY_SOURCE implementation from NetBSD
This is a mostly-unmodified copy of the various *_chk implementations and headers from NetBSD, without yet modifying system headers to start actually including them. A future commit will also apply the needed bits to fix ssp/unistd.h. Reviewed by: imp, pauamma_gundo.com (both previous versions), kib Sponsored by: Stormshield Sponsored by: Klara, Inc. Differential Revision: https://reviews.freebsd.org/D32306
Configuration menu - View commit details
-
Copy full SHA for be04fec - Browse repository at this point
Copy the full SHA be04fecView commit details -
Prepare the system for _FORTIFY_SOURCE
Notably: - libc needs to #undef some of the macros from ssp/* for underlying implementations - ssp/* wants a __RENAME() macro (snatched more or less from NetBSD) There's some extra hinkiness included for read(), since libc spells it as "_read" while the rest of the world spells it "read." Reviewed by: imp, ngie Sponsored by: Stormshield Sponsored by: Klara, Inc. Differential Revision: https://reviews.freebsd.org/D32307
Configuration menu - View commit details
-
Copy full SHA for e555125 - Browse repository at this point
Copy the full SHA e555125View commit details -
Add a build knob for _FORTIFY_SOURCE
In the future, we will Default to _FORTIFY_SOURCE=2 if SSP is enabled, otherwise default to _FORTIFY_SOURCE=0. For now we default it to 0 unconditionally to ease bisect across older versions without the new symbols, and we'll put out a call for testing. include/*.h include their ssp/*.h equivalents as needed based on the knob. Programs and users are allowed to override FORTIFY_SOURCE in their Makefiles or src.conf/make.conf to force it off. Reviewed by: des, markj Relnotes: yes Sponsored by: Stormshield Sponsored by: Klara, Inc. Differential Revision: https://reviews.freebsd.org/D32308
Configuration menu - View commit details
-
Copy full SHA for 9bfd3b4 - Browse repository at this point
Copy the full SHA 9bfd3b4View commit details -
access.2: Mention that lstat(2) should be used for symbolic links
access(), eaccess() and faccessat() will always dereference symbolic links. So add a note in the manual page, that lstat(2) should be used in the case of symbolic links. PR: 262895 Reviewed by: gbe, pauamma_gundo.com MFC after: 1 week Differential Revision: https://reviews.freebsd.org/D44890
Configuration menu - View commit details
-
Copy full SHA for 421025a - Browse repository at this point
Copy the full SHA 421025aView commit details -
User misconfiguration may lead to routing loops where we try to send the tunnel packet into the tunnel. This eventually leads to stack overflows and panics. Avoid this using if_tunnel_check_nesting(), which will drop the packet if we're looping or we hit three layers of nested tunnels. MFC after: 1 week Sponsored by: Rubicon Communications, LLC ("Netgate")
Configuration menu - View commit details
-
Copy full SHA for 59a6666 - Browse repository at this point
Copy the full SHA 59a6666View commit details -
expand: Fix markup for the
-t
option.PR: 274897 Fixes: 8993d78 MFC after: 3 days Reviewed by: gbe Differential Revision: https://reviews.freebsd.org/D45167
Configuration menu - View commit details
-
Copy full SHA for f3eeeb9 - Browse repository at this point
Copy the full SHA f3eeeb9View commit details -
syscalls.master: allow vfork(2) in capsicum(4) capability mode
There is no reason not do do this, we already allow fork(2), and I need vfork(2) for CHERI process colocation. Reviewed by: brooks, emaste, oshogbo MFC after: 1 week Differential Revision: https://reviews.freebsd.org/D39829
Configuration menu - View commit details
-
Copy full SHA for 050555e - Browse repository at this point
Copy the full SHA 050555eView commit details -
src.conf.5: regen after addition of _FORTIFY_SOURCE build knob
Regen to pick up WITHOUT_SSP addition from commit 9bfd3b4. Sponsored by: The FreeBSD Foundation
Configuration menu - View commit details
-
Copy full SHA for b667c40 - Browse repository at this point
Copy the full SHA b667c40View commit details -
Fix the GCC build after _FORTIFY_SOURCE import
We haven't exposed gets(3) in a long time, rip out __gets_chk before it's too late and something builds a gets(3) user with it enabled.
Configuration menu - View commit details
-
Copy full SHA for 8b06826 - Browse repository at this point
Copy the full SHA 8b06826View commit details -
Configuration menu - View commit details
-
Copy full SHA for 6638384 - Browse repository at this point
Copy the full SHA 6638384View commit details -
tmpfs: recalculate OBJ_TMPFS_VREF on reinstantiating node' vnode
Reported and tested by: pho Reviewed by: markj Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45119
Configuration menu - View commit details
-
Copy full SHA for 58d7ac1 - Browse repository at this point
Copy the full SHA 58d7ac1View commit details -
swap-like pagers: assert that writemapping decrease does not pass zero
Reviewed by: markj Tested by: pho Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45119
Configuration menu - View commit details
-
Copy full SHA for 6ada4e8 - Browse repository at this point
Copy the full SHA 6ada4e8View commit details -
tmpfs_destroy_vobject(): clear v_object under the object lock
Which allows tmpfs_pager_writecount_recalc() to reliably detect reclaimed vnode and make its accesses to object->un_pager.swp.private (== vp) safe against reclaim. Note that vnode instantiation already assigns v_object under the object lock. Reviewed by: markj Reported and tested by: pho Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45119
Configuration menu - View commit details
-
Copy full SHA for 4681194 - Browse repository at this point
Copy the full SHA 4681194View commit details -
Configuration menu - View commit details
-
Copy full SHA for e90259a - Browse repository at this point
Copy the full SHA e90259aView commit details -
nvme: Use strlcpy instead of strncpy to ensure termination
Reviewed by: dab, imp Sponsored by: Chelsio Communications Differential Revision: https://reviews.freebsd.org/D45152
Configuration menu - View commit details
-
Copy full SHA for 01fc488 - Browse repository at this point
Copy the full SHA 01fc488View commit details -
nvme/f: Use strlcpy instead of strncpy + manual string termination
Reviewed by: dab, imp Sponsored by: Chelsio Communications Differential Revision: https://reviews.freebsd.org/D45153
Configuration menu - View commit details
-
Copy full SHA for da4230a - Browse repository at this point
Copy the full SHA da4230aView commit details -
nvme_qpair_complete_tracker and nvme_qpair_manual_complete_tracker have to be called without the qpair lock, so assert its unowned. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 5a178b8 - Browse repository at this point
Copy the full SHA 5a178b8View commit details -
nvme: Slight reworking this loop to match FreeBSD style
Update the comment for the code, and slightly rework the code in the 'fast exit' paradigm that FreeBSD generally tries to do. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 9db8ca9 - Browse repository at this point
Copy the full SHA 9db8ca9View commit details -
We don't need to dereference qpair to get the ctrlr pointer each time, so use the cached value. It's not going to change. No change intended. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for c931cf6 - Browse repository at this point
Copy the full SHA c931cf6View commit details -
nvme: Add comment about where tr->deadline is set
It's easy to overlook the chain of events that lead to tr->deadline being updated. Add a comment here to explain what otherwise looks like an oversight w/o careful study. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 0dd84c3 - Browse repository at this point
Copy the full SHA 0dd84c3View commit details -
include: ssp: kill off leftover $FreeBSD$ tag
Most of these were fixed when rebasing the patch forward, but this one seems to have been missed. Reported by: marck Fixes: be04fec ("Import _FORTIFY_SOURCE implementation [...]")
Configuration menu - View commit details
-
Copy full SHA for 0ed58ac - Browse repository at this point
Copy the full SHA 0ed58acView commit details -
These were previously installed by the GCC implementation of libssp, but now they're installed once again with our implementation of FORTIFY_SOURCE. Reported by: jkim Fixes: be04fec ("Import _FORTIFY_SOURCE implementation [...]")
Configuration menu - View commit details
-
Copy full SHA for dec211c - Browse repository at this point
Copy the full SHA dec211cView commit details -
freebsd-tips: Add fortune to find font providing Unicode character
Reviewed by: emaste Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D45183
Configuration menu - View commit details
-
Copy full SHA for 2735824 - Browse repository at this point
Copy the full SHA 2735824View commit details
Commits on May 14, 2024
-
x86: Add Intel TD/HFI related MSR/CPUID defines to specialregs.h
for the coredirector driver. MFC after: 1 week Differential revision: https://reviews.freebsd.org/D44453
Configuration menu - View commit details
-
Copy full SHA for 338d539 - Browse repository at this point
Copy the full SHA 338d539View commit details -
boottrace: Use NULL for SYSINIT's last arg, which is a pointer type
MFC after: 3 days
Configuration menu - View commit details
-
Copy full SHA for d9f1f0a - Browse repository at this point
Copy the full SHA d9f1f0aView commit details -
Intersting/relevant changes since bmake-20240430 ChangeLog since bmake-20240430 2024-05-07 Simon J Gerraty <[email protected]> * VERSION (_MAKE_VERSION): 20240508 Merge with NetBSD make, pick up o make: ensure variables set on command line get added to .MAKEOVERRIDES (even if they start with '.') so they are passed to sub-makes. mk/ChangeLog since bmake-20240430 2024-05-04 Simon J Gerraty <[email protected]> * install-mk (MK_VERSION): 20240504 * dirdeps.mk: allow BUILD_DIRDEPS_OVERRIDES to pass overrides to sub-make building DIRDEPS_CACHE.
Configuration menu - View commit details
-
Copy full SHA for 3c2ab5f - Browse repository at this point
Copy the full SHA 3c2ab5fView commit details -
arm64_pmap: narrow scope of bti_same test
The pmap_bti_same test in pmap_enter_l3c only happens in the !ADDR_IS_KERNEL case; in the other case, a KASSERT fails. So move the test into that case to save a bit of time when ADDR_IS_KERNEL. Reviewed by: andrew Differential Revision: https://reviews.freebsd.org/D45160
Doug Moore authored and Doug Moore committedMay 14, 2024 Configuration menu - View commit details
-
Copy full SHA for b5a1f04 - Browse repository at this point
Copy the full SHA b5a1f04View commit details -
Merge commit '3c2ab5fddc576e58f3ffa70dc5fa95144646a513'
Configuration menu - View commit details
-
Copy full SHA for c9f4001 - Browse repository at this point
Copy the full SHA c9f4001View commit details -
ifconfig: Add format shortcuts.
MFC after: 1 week Reviewed by: imp Differential Revision: https://reviews.freebsd.org/D45166
Configuration menu - View commit details
-
Copy full SHA for 847ef59 - Browse repository at this point
Copy the full SHA 847ef59View commit details -
nuageinit: by default to not enable nuageinit
MFC After: 1 day Reported by: karels@
Configuration menu - View commit details
-
Copy full SHA for 5681636 - Browse repository at this point
Copy the full SHA 5681636View commit details -
Configuration menu - View commit details
-
Copy full SHA for b0b9435 - Browse repository at this point
Copy the full SHA b0b9435View commit details -
Configuration menu - View commit details
-
Copy full SHA for 79bffdf - Browse repository at this point
Copy the full SHA 79bffdfView commit details -
snd_hda: Add patch for Lenovo Ideapad 3
Reported by: [email protected] Sponsored by: The FreeBSD Foundation MFC after: 3 days Reviewed by: emaste Differential Revision: https://reviews.freebsd.org/D45100
Configuration menu - View commit details
-
Copy full SHA for 54cc353 - Browse repository at this point
Copy the full SHA 54cc353View commit details -
snd_hda: Rename LENOVO_I* to LENOVO_IDEAPAD*
Sponsored by: The FreeBSD Foundation MFC after: 3 days Reviewed by: emaste Differential Revision: https://reviews.freebsd.org/D45105
Configuration menu - View commit details
-
Copy full SHA for 2789533 - Browse repository at this point
Copy the full SHA 2789533View commit details -
sound: Remove ncards variable from sound_oss_card_info()
The loop counter is also the card's index, so ncards is redundant. Sponsored by: The FreeBSD Foundation MFC after: 3 days Reviewed by: dev_submerge.ch Differential Revision: https://reviews.freebsd.org/D45144
Configuration menu - View commit details
-
Copy full SHA for 305db91 - Browse repository at this point
Copy the full SHA 305db91View commit details -
ota: Import bsd-feature branch from 20240422 (31bb33a32f71)
The prior import(s) of 2nd edition awk imported the 'main' branch of OTA, not the bsd-feature branch, resulting in a regression for the bsd-specific features. This re-imports those from the correct branch.
Configuration menu - View commit details
-
Copy full SHA for 887b277 - Browse repository at this point
Copy the full SHA 887b277View commit details -
awk: Merge in bsd-feature branch of OTA from 20240422 (31bb33a32f71)
In the last 2nd edition import, I mistakenly grabbed from the 'main' branch of upstream rather than the bsd-feature branch. This means that we have a regression in awk from that point forward: all the BSD-specific bit functions (and a few others) were dropped. This restores it at the same level. MFC After: 1 day Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for eb690a0 - Browse repository at this point
Copy the full SHA eb690a0View commit details -
net80211: add the 802.11-2016 cipher list to the crypto array set.
These are the bitmap / cipher module number fields used for net80211 ciphers. This requires a kernel recompile, but nothing (currently) in userland is using these. Differential Revision: https://reviews.freebsd.org/D44899 Reviewed by: bz, cc
Adrian Chadd authored and Adrian Chadd committedMay 14, 2024 Configuration menu - View commit details
-
Copy full SHA for 05540e6 - Browse repository at this point
Copy the full SHA 05540e6View commit details -
net80211: add placeholder module names for the new ciphers
This is effectively a no-op as we currently don't advertise these ciphers as available anywhere. Note though the intent to support 128 and 256 bit ciphers in the same crypto module. Differential Revision: https://reviews.freebsd.org/D44900 Reviewed by: cc, cy Approved by: cc, cy
Adrian Chadd authored and Adrian Chadd committedMay 14, 2024 Configuration menu - View commit details
-
Copy full SHA for 98e8df9 - Browse repository at this point
Copy the full SHA 98e8df9View commit details -
net80211: allow a single wlan crypto module to register for >1 cipher
This allows a single wlan crypto module to register for more than one cipher. Without it, duplicate linkerset structs are initialised for the actual module loading machinery itself. I've tested this in my private tree with wlan_ccmp providing both 128 and 256 bit cipher support. Differential Revision: https://reviews.freebsd.org/D44901 Reviewed by: bz, cc, cy Approved by: bz, cc, cy
Adrian Chadd authored and Adrian Chadd committedMay 14, 2024 Configuration menu - View commit details
-
Copy full SHA for dcf6ab2 - Browse repository at this point
Copy the full SHA dcf6ab2View commit details -
net80211: add initial key management suites from 802.11-2016, APIs to…
… register them The WPA1/WPA2 driver capabilities aren't really enough in today's world. There are a /lot/ more key management suites to support! So, add initial support for net80211 and drivers to announce what key management suites are supported. These are the list from 802.11-2016 section 9.4.2.25.3 (AKM suites.) The flags are for software supported key management. Drivers may support more key management suites and are welcome to announce more; net80211 will only announce ones that we know net80211 knows "enough" about to support correctly. There /are/ other suites that may be interesting to some people in the future that are not part of this set - eg if anyone ever wants to support the Chinese WAPI standard - so this bitmap is not specifically just the AKM suites in the RSN OUI. This should eventually be communicated up to the wpa_supplicant and hostapd via a replacement driver/vap capabilities call so they know what to enable rather than just IEEE80211_C_WPA1 / IEEE80211_C_WPA2. Differential Revision: https://reviews.freebsd.org/D44919 Reviewed by: bz
Adrian Chadd authored and Adrian Chadd committedMay 14, 2024 Configuration menu - View commit details
-
Copy full SHA for c7f5f14 - Browse repository at this point
Copy the full SHA c7f5f14View commit details -
AMD CPUs: update bits and data from CPUID 0x8000_0008
from AMD APM vol3 doc no 24594 Rev. 3.36 March 2024 Reviewed and tested by: emaste Sponsored by: Advanced Micro Devices (AMD) Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45188
Configuration menu - View commit details
-
Copy full SHA for c6113ac - Browse repository at this point
Copy the full SHA c6113acView commit details -
ssp: appease -Wgnu-statement-expression-from-macro-expansion
It's a stupid warning, but some ports enable it by default and were already defining _FORTIFY_SOURCE, thus exposing the new macros immediately. This at least fixes the libfido2 build, perhaps others as well. While we're here, fix a fresh build of stand w/ FORTIFY_SOURCE enabled by not pulling in the ssp headers if _STANDALONE is defined. We do not have runtime support in libsa as of the time of writing. Reported by: netchild Sponsored by: Stormshield Sponsored by: Klara, Inc.
Configuration menu - View commit details
-
Copy full SHA for 5af6fbd - Browse repository at this point
Copy the full SHA 5af6fbdView commit details
Commits on May 15, 2024
-
Enable soft updates by default for UFS2 filesystems.
Soft updates dramatically improve the performance of UFS filesystems. The newfs(8) utility currently does not enable them by default. The FreeBSD installer enables soft updates by default. However custom built installations that do not specify the -U option to newfs(8) and the prebuilt UFS system images get filesystems without soft updates enabled. There are several testing sites that run benchmarks comparing the performance of Linux distributions versus BSD distributions. When they run filesystem comparison benchmarks they use newfs(8) to create the UFS filesystem. Because it does not have soft updates enabled it runs poorly versus the Linux ext4 filesystem. When I have suggested to them that they should enable soft updates on the UFS filesystem in their testing their response is that they expect the utility that creates the filesystem to use optimal defaults and that they cannot be expected to fiddle with various option settings. The purpose of this change is to give a filesystem created with newfs(8) reasonably optimal settings. For UFS2 this means enabling soft updates. For UFS1 which tends to be used on small systems with minimal memory and CPU speed, the lower memory footprint of running without soft updates is a more sensible default. This change adds a note in the section of the newfs(8) manual page that describes the -U option for enabling soft updates that they are enabled by default for UFS2 filesystems and that they can be disabled by using tunefs(8). Reviewed-by: Warner Losh, kib MFC after: 1 week Differential Revision: https://reviews.freebsd.org/D45201
Kirk McKusick authored and Kirk McKusick committedMay 15, 2024 Configuration menu - View commit details
-
Copy full SHA for 61dece6 - Browse repository at this point
Copy the full SHA 61dece6View commit details -
Issue CTSRD-CHERI#237 : Resolver uses nameserver commented out in /et…
…c/resolv.conf This /etc/resolv.conf: # x # nameserver 8.8.8.8 Still configured 8.8.8.8 as nameserver, because the comment detection in `ldns_resolver_new_frm_fp_l()` didn't anticipate empty lines before the comment. This fix removed all comment handling from `ldns_resolver_new_frm_fp_l()`. Instead a new function is introduced `ldns_fget_token_l_resolv_conf()` that skips comments that start with '#' and ';'. The old `ldns_fget_token_l()` (that is used for zonefiles too) still accepts only ';' for comments.
Configuration menu - View commit details
-
Copy full SHA for 0c57cb2 - Browse repository at this point
Copy the full SHA 0c57cb2View commit details -
Issue CTSRD-CHERI#237 : Resolver uses nameserver commented out in /et…
…c/resolv.conf This /etc/resolv.conf: # x # nameserver 8.8.8.8 Still configured 8.8.8.8 as nameserver, because the comment detection in `ldns_resolver_new_frm_fp_l()` didn't anticipate empty lines before the comment. This fix removed all comment handling from `ldns_resolver_new_frm_fp_l()`. Instead a new function is introduced `ldns_fget_token_l_resolv_conf()` that skips comments that start with '#' and ';'. The old `ldns_fget_token_l()` (that is used for zonefiles too) still accepts only ';' for comments.
Configuration menu - View commit details
-
Copy full SHA for b5fb1f4 - Browse repository at this point
Copy the full SHA b5fb1f4View commit details -
atf: Guard against multiple evaluation.
Note that the ATF-C++ macros have the same issue, but they are not as easily fixed. MFC after: 3 days Reviewed by: ngie Differential Revision: https://reviews.freebsd.org/D45148
Configuration menu - View commit details
-
Copy full SHA for a7beca6 - Browse repository at this point
Copy the full SHA a7beca6View commit details -
Revert "Issue CTSRD-CHERI#237 : Resolver uses nameserver commented ou…
…t in /etc/resolv.conf" This reverts commit b5fb1f4.
Configuration menu - View commit details
-
Copy full SHA for 154ad8e - Browse repository at this point
Copy the full SHA 154ad8eView commit details -
Configuration menu - View commit details
-
Copy full SHA for 4891157 - Browse repository at this point
Copy the full SHA 4891157View commit details -
ldns: Ignore commented-out lines in resolv.conf.
This merges upstream PR 238 + an additional bug fix. PR: 278721 MFC after: 1 week
Configuration menu - View commit details
-
Copy full SHA for 3b092e4 - Browse repository at this point
Copy the full SHA 3b092e4View commit details -
adduser: Additional variable fixes.
One function used `_input` without making it local, causing its value to leak into other functions. This broke the `-f` case. Fix that instance and initialize all local variables that weren't already initialized. Fixes: 170d088 MFC after: 3 days Reviewed by: karels Differential Revision: https://reviews.freebsd.org/D45204
Configuration menu - View commit details
-
Copy full SHA for 46a619c - Browse repository at this point
Copy the full SHA 46a619cView commit details -
MFC after: 3 days Reviewed by: imp, allanjude Differential Revision: https://reviews.freebsd.org/D45209
Configuration menu - View commit details
-
Copy full SHA for 42b28f8 - Browse repository at this point
Copy the full SHA 42b28f8View commit details -
freebsd-tips: Tweak fortune to find font providing Unicode character
While here, remove my name and email address. Reported by: bapt Sponsored by: The FreeBSD Foundation
Configuration menu - View commit details
-
Copy full SHA for ea3751f - Browse repository at this point
Copy the full SHA ea3751fView commit details -
uart: Honour clock-frequency in FDT for UART_FDT_CLASS if present
The StarFive VisionFive 2 has a Synopsys DesignWare ABP UART, whose driver uses UART_FDT_CLASS rather than UART_FDT_CLASS_AND_DEVICE as it has its own separate newbus driver. This UART is driven by a 24MHz clock as specified in the FDT, but we don't currently look at the property here, instead passing down 0 and letting the default value be used in the 8250 driver (~1.8MHz). As a result the divisor is misconfigured for the current baud rate for the entire kernel boot process. Once the newbus driver attaches the correct frequency is saved in the softc, but that does not take effect until the next time ns8250_param is called and the divisor is recalculated, namely when userspace runs and /dev/console is opened (note that ns8250_init does not get called when the newbus device corresponding to the current console attaches). Fix this issue by attemmpting to get the current clock frequency as for the UART_FDT_CLASS_AND_DEVICE_CASE, but falling back to 0 rather than failing on error. Reviewed by: imp, mhorne Differential Revision: https://reviews.freebsd.org/D45159
Configuration menu - View commit details
-
Copy full SHA for fc59fc3 - Browse repository at this point
Copy the full SHA fc59fc3View commit details -
riscv: fix L0 PTE setup (Sv48)
Per the Privilege Spec, the Accessed (A) or Dirty (D) bits must only be set for a leaf PTE. It seems newer versions of QEMU have started to enforce this requirement, and without this change, pmap_bootstrap() hangs when switching to Sv48 mode. Reviewed by: jrtc27, markj MFC after: 3 days Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D45210
Configuration menu - View commit details
-
Copy full SHA for d7adf3b - Browse repository at this point
Copy the full SHA d7adf3bView commit details
Commits on May 16, 2024
-
vfs_domount_update(): style, use space instead of tab
Noted by: mckusick Sponsored by: The FreeBSD Foundation MFC after: 3 days
Configuration menu - View commit details
-
Copy full SHA for 5a061a3 - Browse repository at this point
Copy the full SHA 5a061a3View commit details -
vfs_domount_update(): postpone setting MNT_UNION until VFS_MOUNT() is…
… done The file system that handles updating the mount point might do lookups during the update, in which case it could find the flag MNT_UNION set on the mp while mount point is still not updated. In particular, the rootvp->v_mount->mnt_vnodecovered is not yet set. Delay setting MNT_UNION until the mount is performed. PR: 265311 Reported by: Robert Morris <[email protected]> Reviewed by: mckusick, olce Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45208
Configuration menu - View commit details
-
Copy full SHA for 21ccdb4 - Browse repository at this point
Copy the full SHA 21ccdb4View commit details -
linuxkpi: spinlock: Simplify code
Just use a typedef for spinlock_t, no need to create a useless structure. Reviewed by: bz, emaste Sponsored by: Beckhoff Automation GmbH & Co. KG Differential Revision: https://reviews.freebsd.org/D45205
Configuration menu - View commit details
-
Copy full SHA for ae38a1a - Browse repository at this point
Copy the full SHA ae38a1aView commit details -
linuxkpi: rwlock: Simplify code
Just use a typedef for rwlock_t, no need to create a useless structure. Reviewed by: bz Sponsored by: Beckhoff Automation GmbH & Co. KG Differential Revision: https://reviews.freebsd.org/D45206
Configuration menu - View commit details
-
Copy full SHA for 5c0a192 - Browse repository at this point
Copy the full SHA 5c0a192View commit details -
linuxkpi: refcount: Use atomic_t directly
Simply use a typedef for refcount_t on atomic_t, this allow us to use a nativ type and also changing struct kref to directly use a refcount_t like Linux. Reviewed by: bz Sponsored by: Beckhoff Automation GmbH & Co. KG Differential Revision: https://reviews.freebsd.org/D45207
Configuration menu - View commit details
-
Copy full SHA for abb1a13 - Browse repository at this point
Copy the full SHA abb1a13View commit details -
contrib/bsddialog: Import version 1.0.2
Implicitly import also 1.0.1, both versions are for fixing and feature requests. Fixing: Change --mixedform behavior to fix a bsdinstall fault avoiding to change the command line in wlanconfig. Feature requests: * Add keys to navigate menus. * Add key to redraw dialogs. * Avoid to handle env NCURSES_NO_UTF8_ACS in PuTTY. See '2024-04-11 Version 1.0.2' and '2023-11-16 Version 1.0.1' in /usr/src/contrib/bsddialog/CHANGELOG for more detailed information. PR: 274472 Differential Revision: D42380
Configuration menu - View commit details
-
Copy full SHA for be8846b - Browse repository at this point
Copy the full SHA be8846bView commit details -
contrib/bsddialog: Import version 1.0.2
Implicitly import also 1.0.1, both versions are for fixing and feature requests. Fixing: Change --mixedform behavior to fix a bsdinstall fault avoiding to change the command line in wlanconfig. Feature requests: * Add keys to navigate menus. * Add key to redraw dialogs. * Avoid to handle env NCURSES_NO_UTF8_ACS in PuTTY. See '2024-04-11 Version 1.0.2' and '2023-11-16 Version 1.0.1' in /usr/src/contrib/bsddialog/CHANGELOG for more detailed information. PR: 274472 Differential Revision: D42380 Merge commit 'be8846bd9e069f4a6bea3d769005bea96cf43990'
Configuration menu - View commit details
-
Copy full SHA for a6d8be4 - Browse repository at this point
Copy the full SHA a6d8be4View commit details -
man filesystems: move driver pages to section four
Filesystem manual pages describe drivers, not formats; except for fs, which describes the structures of ffs/ufs, not how to use it in the system. Reported by: emaste Reviewed by: des, imp, meena (previous version) Pull Request: freebsd/freebsd-src#1077
Configuration menu - View commit details
-
Copy full SHA for 1687d77 - Browse repository at this point
Copy the full SHA 1687d77View commit details -
man filesystems: ObsoleteFiles after move to sec 4
Reported by: imp Reviewed by: des, imp Pull Request: freebsd/freebsd-src#1077
Configuration menu - View commit details
-
Copy full SHA for a03e8a4 - Browse repository at this point
Copy the full SHA a03e8a4View commit details -
man filesystems: fix xrefs after move to section 4
Reviewed by: des, imp Pull Request: freebsd/freebsd-src#1077
Configuration menu - View commit details
-
Copy full SHA for 1a720cb - Browse repository at this point
Copy the full SHA 1a720cbView commit details -
netstat(1): increase width of Netif column
The previous width of Netif (10 or 8) was too short for modern interface names; make it 12, which is long enough to display "epair0a.1000". This came up in practice with genet(4) interfaces, since the base interface name is long enough that with the previous limit, VLAN identifiers would be truncated at 1 character in the IPv6 output: "genet0.100" becomes "genet0.1". The width is now fixed, and doesn't depend on the address family, because there's no reason that length of the interface name would vary based on the AF. Reviewed by: imp,zlei,Mina Galić Pull Request: freebsd/freebsd-src#1223
Configuration menu - View commit details
-
Copy full SHA for d33b87e - Browse repository at this point
Copy the full SHA d33b87eView commit details -
netstat(8): for -W, use IFNAMSIZ
If -W is specified, use IFNAMSIZ as the width of the Netif column, instead of the default 12. Reviewed by: imp,zlei,Mina Galić Pull Request: freebsd/freebsd-src#1223
Configuration menu - View commit details
-
Copy full SHA for ae9c0ba - Browse repository at this point
Copy the full SHA ae9c0baView commit details -
sys/modules/dpdk_lpm4: do not build without INET
Reviewed by: imp Pull Request: freebsd/freebsd-src#1236
Configuration menu - View commit details
-
Copy full SHA for 304a032 - Browse repository at this point
Copy the full SHA 304a032View commit details -
In bhyve_parse_config_option(), a string is allocated and passed to nvlist_add_string() but not free'd afterwards. Reported by: Coverity CID: 1544049 Sponsored by: The FreeBSD Foundation Reviewed by: imp Pull Request: freebsd/freebsd-src#1234
Configuration menu - View commit details
-
Copy full SHA for 1787871 - Browse repository at this point
Copy the full SHA 1787871View commit details -
The str variable in cctl_nvlist_end_element() does not get free()'d when converted to an integer value. (name is "trtype") Reported by: Coverity Scan Coverity ID: 1545039 Sponsored by: The FreeBSD Foundation Reviewed by: imp Pull Request: freebsd/freebsd-src#1237
Configuration menu - View commit details
-
Copy full SHA for f381173 - Browse repository at this point
Copy the full SHA f381173View commit details -
makeman: extend duplicate option warning to OPT_ options
In a local tree I accidentally had OPT_INIT_ALL defaulting to zero in userland and none in kernel. This resulted in the INIT_ALL text appearing twice in src.conf.5. Reviewed by: brooks Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D45184
Configuration menu - View commit details
-
Copy full SHA for 65fd76b - Browse repository at this point
Copy the full SHA 65fd76bView commit details -
linuxkpi: Provide a non-NULL value for THIS_MODULE
THIS_MODULE is used to differentiate modules on Linux. We currently completely stub out any Linux struct module usage, but THIS_MODULE is still used to populate the "owner" fields of various drivers. Even though we don't actually dereference these "owner" fields they are still used by drivers to check if devices/dmabufs/etc come from different modules. For example, during DRM GEM import some drivers check if the dmabuf's owner matches the dev's owner. If they match because they are both NULL drivers may incorrectly think two resources come from the same module. This adds a general purpose __this_linker_file which will point to the linker file of the module that uses it. We can then use that pointer to have a valid value for THIS_MODULE. Reviewed by: bz, jhb Differential Revision: https://reviews.freebsd.org/D44306
Configuration menu - View commit details
-
Copy full SHA for 28a5910 - Browse repository at this point
Copy the full SHA 28a5910View commit details -
SysV SHM: move SHMSEG constants to sys/shm.h
There are planned consumers in linprocfs. Tested by: Ricardo Branco <[email protected]> Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45175
Configuration menu - View commit details
-
Copy full SHA for 5372516 - Browse repository at this point
Copy the full SHA 5372516View commit details -
SysV IPC: provide in-kernel helpers to obtain ipcs(8)-like information
PR: 278949 Reviewed by: markj Tested by: Ricardo Branco <[email protected]> Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45175
Configuration menu - View commit details
-
Copy full SHA for 87a1565 - Browse repository at this point
Copy the full SHA 87a1565View commit details -
libcapsicum: document return values
Reviewed by: emaste Requested by: des Differential Revision: https://reviews.freebsd.org/D45222
Configuration menu - View commit details
-
Copy full SHA for 3cb6c6c - Browse repository at this point
Copy the full SHA 3cb6c6cView commit details -
Merge commit 87f3407856e6 from llvm-project (by Phoebe Wang):
[X86][Driver] Do not add `-evex512` for `-march=native` when the target doesn't support AVX512 (#91694) This prevents problems with ports that fail to build with CPUTYPE=native, if the native CPU supports AVX512F, resulting in errors like: /wrkdirs/usr/ports/archivers/libdeflate/work/libdeflate-1.20/lib/x86/adler32_template.h:197:21: error: always_inline function '_mm512_set1_epi8' requires target feature 'evex512', but would be inlined into function 'adler32_x86_avx512_vl512_vnni' that is compiled without support for 'evex512' 197 | const vec_t ones = VSET1_8(1); | ^ /wrkdirs/usr/ports/archivers/libdeflate/work/libdeflate-1.20/lib/x86/adler32_template.h:116:23: note: expanded from macro 'VSET1_8' 116 | # define VSET1_8(a) _mm512_set1_epi8(a) | ^ /wrkdirs/usr/ports/archivers/libdeflate/work/libdeflate-1.20/lib/x86/adler32_template.h:197:21: error: AVX vector return of type '__m512i' (vector of 8 'long long' values) without 'evex512' enabled changes the ABI /wrkdirs/usr/ports/archivers/libdeflate/work/libdeflate-1.20/lib/x86/adler32_template.h:116:23: note: expanded from macro 'VSET1_8' 116 | # define VSET1_8(a) _mm512_set1_epi8(a) | ^ Ports known to be affected are: archivers/libdeflate, devel/highway, www/node20, and lang/rust. (For rust itself there is also a similar issue reported at rust-lang/rust#121088). PR: 276104 Reported by: netchild MFC after: 3 days
Configuration menu - View commit details
-
Copy full SHA for fcfb2d6 - Browse repository at this point
Copy the full SHA fcfb2d6View commit details -
Trim a spurious trailing backslash
Reported by: dim Fixes: 1687d77 man filesystems: move driver pages to section four
Configuration menu - View commit details
-
Copy full SHA for 7552991 - Browse repository at this point
Copy the full SHA 7552991View commit details
Commits on May 17, 2024
-
Some linux code re-init some spinlock so add MTX_NEW to mtx_init. Reported by: David Wolfskill <[email protected]> Fixes: ae38a1a ("linuxkpi: spinlock: Simplify code")
Configuration menu - View commit details
-
Copy full SHA for cff79fd - Browse repository at this point
Copy the full SHA cff79fdView commit details -
linuxkpi: rwlock: Fix rwlock_init
Some linux code re-init some spinlock so add MTX_NEW to mtx_init. Reported by: rlibby Fixes: 5c0a192 ("linuxkpi: rwlock: Simplify code")
Configuration menu - View commit details
-
Copy full SHA for a7b222d - Browse repository at this point
Copy the full SHA a7b222dView commit details -
rtld: Add MD_OBJ_ENTRY to extend Struct_Obj_Entry
Add a macro the architectures can use to add per-arch fields to Struct_Obj_Entry. Reviewed by: kib Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45116
Configuration menu - View commit details
-
Copy full SHA for 06db20f - Browse repository at this point
Copy the full SHA 06db20fView commit details -
This will be used to handle the DT_AARCH64_VARIANT_PCS tag. Reviewed by: kib Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45117
Configuration menu - View commit details
-
Copy full SHA for dd4155b - Browse repository at this point
Copy the full SHA dd4155bView commit details -
rtld: Add support for arm64 variant pcs
The aarch64 ELF spec has support for a variant of the normal procedure call standard that doesn't follow the normal register convention, e.g. using more registers as arguments, or different register state is preserved. Add support to rtld to handle this. As we don't know which registers need to be preserved disable lazy binding for these functions. Reviewed by: kib Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D44869
Configuration menu - View commit details
-
Copy full SHA for d51fa0a - Browse repository at this point
Copy the full SHA d51fa0aView commit details -
rtld: Add arm64 variant pcs tests
When marking a function as variant pcs we can use registers not normally used in procedure calls. Add a test that uses this and stores all general purpose registers to a buffer and compare this buffer with the expected value later. Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D44870
Configuration menu - View commit details
-
Copy full SHA for 9e48c30 - Browse repository at this point
Copy the full SHA 9e48c30View commit details -
rtld: Move powerpc specific code to powerpc files
There are two variables set by dynamic tags in the powerpc runtime linker. Now we have a way to split out architecture-specific dynamic tags use it to handle these. Reviewed by: kib, jhibbits Obtained from: jhibbits (earlier version) Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45182
Configuration menu - View commit details
-
Copy full SHA for 1cd90a2 - Browse repository at this point
Copy the full SHA 1cd90a2View commit details -
arm64: Add MRS_REG_ALT_NAME ID register macros
These can be used even when the compiler is too old for the register to be included. Reviewed by: Zachary Leaf <[email protected]> Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45176
Configuration menu - View commit details
-
Copy full SHA for d6d860c - Browse repository at this point
Copy the full SHA d6d860cView commit details -
arm64: Use the _REG macros to read ID registers
To build with old toolchains use the *_REG macros to access the ID registers. These become a name in the form S?_?_C?_C?_? where the '?' values encode the op and CR values needed to access the register. For consistency use these macros for all ID registers, even if most toolchains understand them. Reviewed by: Zachary Leaf <[email protected]> Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45177
Configuration menu - View commit details
-
Copy full SHA for cd36810 - Browse repository at this point
Copy the full SHA cd36810View commit details -
Revert "rtld: Add arm64 variant pcs tests"
It's missing an mtree update This reverts commit 9e48c30.
Configuration menu - View commit details
-
Copy full SHA for 2228d7c - Browse repository at this point
Copy the full SHA 2228d7cView commit details -
arm64/vmm: Fix the build with GCC
- Fix the spelling of handle_el2_el1_irq64 - Add .section before .rodata as the GCC build needs it Sponsored by: Arm Ltd
Configuration menu - View commit details
-
Copy full SHA for 4660d96 - Browse repository at this point
Copy the full SHA 4660d96View commit details -
dd a missing underscore to arm_smccc_1_2_* to fix the GCC build. Sponsored by: Arm Ltd
Configuration menu - View commit details
-
Copy full SHA for 2790ff2 - Browse repository at this point
Copy the full SHA 2790ff2View commit details -
arm64: make SPE regs use ALT_NAME macro
When the register is not defined in Armv8.0 i.e. added in a later extension, like SPE added in v8.2, the alternative name format of: S<op0>_<op1>_C<crn>_C<crm>_<op2> should be used; otherwise, calls to {READ,WRITE}_SPECIALREG() will fail. Use the MRS_REG_ALT_NAME() macro for SPE changing hex to decimal as required by the macro. Reviewed by: andrew Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45171
Configuration menu - View commit details
-
Copy full SHA for f7bdaa1 - Browse repository at this point
Copy the full SHA f7bdaa1View commit details -
arm64: add PMBSR_MSS_{BSC,FSC} status code field
Bits [5:0] of PMBSR_MSS encodes either Buffer Status Code (BSC) or Fault Status Code (FSC) depending on PMBSR_EC value. Add PMBSR_MSS_{BSC,FSC} to cover this field. Reviewed by: andrew Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45172
Configuration menu - View commit details
-
Copy full SHA for 10b3eac - Browse repository at this point
Copy the full SHA 10b3eacView commit details -
CONTEXTIDR_EL1 is used in debug and trace features to identify the current process or context. Reviewed by: andrew Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45173
Configuration menu - View commit details
-
Copy full SHA for 4f8ba1c - Browse repository at this point
Copy the full SHA 4f8ba1cView commit details -
aarch64: disable LIB32 with gcc
gcc doesn't have -m32 support on aarch64 so mark LIB32 broken there. We have to check both COMPILER_TYPE and X_COMPILER_TYPE becuase X_COMPILER_TYPE is only conditionally set and COMPILER_TYPE is the host compiler in Makefile.inc1. Reviewed by: emaste Differential Revision: https://reviews.freebsd.org/D45089
Configuration menu - View commit details
-
Copy full SHA for 16d8dfd - Browse repository at this point
Copy the full SHA 16d8dfdView commit details -
Since at least 2022 (see https://reviews.freebsd.org/D36754), it has not been possible to build armv6/armv7 with gcc due to atomics macros gcc doesn't like. Prevent developers doing due diligance from wasting time and CPU cycles on this combination as it just fails to build in libc. Reviewed by: imp, andrew Differential Revision: https://reviews.freebsd.org/D45193
Configuration menu - View commit details
-
Copy full SHA for 4c0dfd5 - Browse repository at this point
Copy the full SHA 4c0dfd5View commit details -
zfs: Avoid a gcc -Wint-to-pointer-cast warning
On 32-bit platforms long long is generally 64-bits. Sufficiently modern versions of gcc (13 in my testing) complains when casting a pointer to an integer of a different width so cast to uintptr_t first to avoid the warning. Fix i386 gcc builds while we wait for this to be merged to OpenZFS. Sponsored by: DARPA, AFRL Pull Request: openzfs/zfs#16203
Configuration menu - View commit details
-
Copy full SHA for d316de2 - Browse repository at this point
Copy the full SHA d316de2View commit details -
uart: DBG2 support to find the debug uart
The Debug Port Table 2 (DBG2) contains information on which devices can be used for debugging purposes. Add support to the uart driver to use the DBG2 table when enabled from loader. Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D44359
Configuration menu - View commit details
-
Copy full SHA for 097bd33 - Browse repository at this point
Copy the full SHA 097bd33View commit details -
arm: Add a missing interrupt to the generic timer
The ACPI generic timer attachment added 3 interrupts, but missed the hypervisor physical interrupt. As the field is present in all versions of the GTDT ACPI table and isn't an optional interrupts we can add it to the interrupts provided to the driver. Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D43974
Configuration menu - View commit details
-
Copy full SHA for f715e95 - Browse repository at this point
Copy the full SHA f715e95View commit details -
arm: Use the correct irq when in the hypervisor
When booting in the hypervisor state we need to use the hypervisor interrupt in the generic timer. In this case the registers we access in the kernel are remapped to the EL2 versions, however this causes an unexpected interrupt to trigger. Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D43975
Configuration menu - View commit details
-
Copy full SHA for e72c417 - Browse repository at this point
Copy the full SHA e72c417View commit details -
arm64: Support break and watch points in VHE
When booting the kernel with VHE it will be running at EL2. The current config register values only enable the reaces at EL1 when tracing the kernel. Set the HMC flag to also trap from EL2. Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45121
Configuration menu - View commit details
-
Copy full SHA for 457fa0f - Browse repository at this point
Copy the full SHA 457fa0fView commit details -
fib_dxr: check if cached fib_data matches the new request in dxr_init()
When calling dxr_init(), the FIB_ALGO infrastructure may provide a pointer to a previous dxr instance, which permits reuse of auxiliary dxr structures, i.e. incremental lookup structure updates. For dxr this is a crucial feature provided by FIB_ALGO, since dxr incremental updates are typically several orders of magnitude faster than full lookup table rebuilds. However, the auxiliary dxr structure caches a pointer to struct fib_data and relies upon it for performing incremental updates. Apparently, incremental rebuild requests from FIB_ALGO, i.e. a calls to dxr_init() with a pointer old_data set, may (under not yet fully understood circumstances) be invoked within a different fib_data context than the one cached in the previous version of dxr auxiliary structures. In such (rare) events, we ignore the offered old dxr context, and proceed with a full lookup structure rebuild instead of attempting an incremental one using a fib_data context which may or may not no longer be valid, and thus lead to a system crash. PR: 278422 MFC after: 1 week
Configuration menu - View commit details
-
Copy full SHA for 4ab122e - Browse repository at this point
Copy the full SHA 4ab122eView commit details -
bhyve: avoid resource leak in error path
In e820_finalize(), the e820_fwcfg_item variable, containing the etc/e820 file (for the e820 table from the BIOS) is not free()'d when it could not be added to the QEMU firmware configuration device (fw_cfg). Reported by: Coverity Scan CID: 1522761 Reviewed by: corvink, jhb Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D45223
Configuration menu - View commit details
-
Copy full SHA for e9806d2 - Browse repository at this point
Copy the full SHA e9806d2View commit details -
fib_dxr: do not leak memory if FIB constellation hits structural limit
DXR lookup table encoding has an inherent structural limit on the amount of binary search ranges it can accomodate. With the current IPv4 BGP views (circa 1 M prefixes) and default DXR encoding we are only at around 5% of that limit, so far, far away from hitting it. Just in case it ever gets hit, make sure we free the allocated structures, instead of leaking it. MFC after: 1 week
Configuration menu - View commit details
-
Copy full SHA for 19bd24c - Browse repository at this point
Copy the full SHA 19bd24cView commit details -
fib_dxr: code hygiene, prune old code, no functional changes
The !DXR2 code corresponds to the original DXR encoding proposal from 2012 with a single direct-lookup stage, which is inferior to the more recent (DXR2) variant with two-stage trie both in terms of memory footprint of the lookup structures, and in terms of overall lookup througput. I'm axing the old code chunks to (hopefully) somewhat improve readability, as well as to simplify future maintenance and updates. MFC after: 1 week
Configuration menu - View commit details
-
Copy full SHA for 42b3c16 - Browse repository at this point
Copy the full SHA 42b3c16View commit details -
tpm: Add new tpm_bus.c to module Makefile
Reported by: eduardo@ Fixes: c2e9c5b ("tpm: Refactor TIS and add a SPI attachment")
Configuration menu - View commit details
-
Copy full SHA for 62adeb9 - Browse repository at this point
Copy the full SHA 62adeb9View commit details -
libgcc_s: fix nonsense defines
These symbols are present on amd64 or i386. Reported by: kaktus, jhibbits Fixes: 98c8caa libgcc_s: 80-bit long double function are x86-only
Configuration menu - View commit details
-
Copy full SHA for 25db7bd - Browse repository at this point
Copy the full SHA 25db7bdView commit details -
bhyve: avoid side effect in assertion
An assert() was setting the error variable instead of checking it. Reported by: Coverity Scan CID: 1521431 Reviewed by: jhb Sponsored by: The FreeBSD Foundation Pull Request: freebsd/freebsd-src#1244
Configuration menu - View commit details
-
Copy full SHA for f7d45c5 - Browse repository at this point
Copy the full SHA f7d45c5View commit details -
libcxxrt: allow build with gcc13 and --no-undefined-version
GCC 13 supports _Float16 and __int128 on fewer architectures than clang and thus libcxxrt compiled with gcc13 is sometimes missing related symbols. Hack around this by explicitly appending --undefined-version to LDFLAGS in problematic cases. Reviewed by: theraven, dim Differential Revision: https://reviews.freebsd.org/D45233
Configuration menu - View commit details
-
Copy full SHA for 1062db3 - Browse repository at this point
Copy the full SHA 1062db3View commit details -
Mark powerpc* and riscv broken. Refactor and add a TRY_GCC_BROKEN option to build anyway. This simplifies things for people trying to get gcc builds working while letting other developers know that they aren't expected to work. Reviewed by: jhb, emaste Improves: 4c0dfd5 arm: fail early on gcc builds Differential Revision: https://reviews.freebsd.org/D45230
Configuration menu - View commit details
-
Copy full SHA for 61ad1dd - Browse repository at this point
Copy the full SHA 61ad1ddView commit details -
cxgbe(4): sc->port is indexed by port_id and not tx_chan.
MFC after: 1 week Sponsored by: Chelsio Communications
Configuration menu - View commit details
-
Copy full SHA for cca3506 - Browse repository at this point
Copy the full SHA cca3506View commit details -
cxgbe(4): Consolidate all mk_set_tcb_field_ulp in one place.
MFC after: 1 week Sponsored by: Chelsio Communications
Configuration menu - View commit details
-
Copy full SHA for 64a00f8 - Browse repository at this point
Copy the full SHA 64a00f8View commit details
Commits on May 18, 2024
-
PR: 278988 Reviewed by: bapt Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D45220
Configuration menu - View commit details
-
Copy full SHA for fb623aa - Browse repository at this point
Copy the full SHA fb623aaView commit details
Commits on Aug 29, 2024
-
arm64: add page-to-pte convenience macros
Define macros to perform pte to vm_page and vm_page to pte conversions without composing two macros, and use the convenience macros wherever possible. Reviewed by: alc Differential Revision: https://reviews.freebsd.org/D44699
Configuration menu - View commit details
-
Copy full SHA for 50bba03 - Browse repository at this point
Copy the full SHA 50bba03View commit details -
tcp rack: improve handling of front states
When the RACK stack wants to send a FIN, but still has outstanding or unsent data, it sends a challenge ack. Don't do this when the TCP endpoint is still in the front states, since it does not make sense. Reviewed by: rrs MFC after: 3 days Sponsored by: Netflix, Inc. Differential Revision: https://reviews.freebsd.org/D45122
Configuration menu - View commit details
-
Copy full SHA for b3edfa9 - Browse repository at this point
Copy the full SHA b3edfa9View commit details -
nvme: Add telemetry page definitions
Add definition for page types 7 and 8 for host initiated telemetry and controller initiated telemetry (they differ by one byte, but that byte that's defined in the host version is reserved in the controller version). Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 1940baa - Browse repository at this point
Copy the full SHA 1940baaView commit details -
nvmecontrol: Implement telemetry-log command.
This produces the same data as the Linux nvme-cli 'nvme telemetry-log' command. It extracts the telemetry log from drive. This is a variable length log, so we read the first page and find out how much of the log to grab. There's 3 levels of details available, and we grab the level of detail specified on the command line. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for d514783 - Browse repository at this point
Copy the full SHA d514783View commit details -
stand: Spell LUA_COMPILE_SET correctly.
MFC After: 2 days Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for e7ebde4 - Browse repository at this point
Copy the full SHA e7ebde4View commit details -
nvmecontrol: Appease a meaningless signed error warning thing
Consistently use the weird ssize_t type for things I know are unsigned, but which none-the-less need to be compared to signed things to prevent a bogus warning. Sigh, these aren't bugs, can't possibly be bugs and a waste of time to fix. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for e1f4a4d - Browse repository at this point
Copy the full SHA e1f4a4dView commit details -
/bin/rmdir: Exit with status 2 for invalid arguments
PR: 277677 Signed-off-by: Henrich Hartzer <[email protected]> Reviewed by: imp Pull Request: freebsd/freebsd-src#1161
Configuration menu - View commit details
-
Copy full SHA for c39034c - Browse repository at this point
Copy the full SHA c39034cView commit details -
In some cases, the USB_QUIRK_VP macro was being misused. Instead of setting quirks to the intended value, the first two supplied quirks would go into lo_rev and hi_rev. Replace it with USB_QUIRK_VO which only takes the needed args. This also makes the Dummy products, which where being used to correctly set vendor only quirks, not necessary. Reviewed by: imp Pull Request: freebsd/freebsd-src#1153
Configuration menu - View commit details
-
Copy full SHA for d422b16 - Browse repository at this point
Copy the full SHA d422b16View commit details -
usb: Remove uneeded revision verbosity from quirks list
Seperate usb quirks that target specific revisions from those that dont. Alot of the quirks dont use lo_rev and hi_rev, so we can abstract the 0x0000, 0xffff into a macro. [[ This commit is a bit more churn than we like. I carefully reviewed each one and they are all good. The end product is better -- imp ]] Reviewed by: imp Pull Request: freebsd/freebsd-src#1153
Configuration menu - View commit details
-
Copy full SHA for 4b6f251 - Browse repository at this point
Copy the full SHA 4b6f251View commit details -
linprocfs: Add support for proc/sysvipc/{msg,sem,shm}
Signed-off-by: Ricardo Branco <[email protected]> Reviewed by: imp Pull Request: freebsd/freebsd-src#1218
Configuration menu - View commit details
-
Copy full SHA for ae55575 - Browse repository at this point
Copy the full SHA ae55575View commit details -
linux: Make module standalone-buildable
Add opt_inet.h and opt_usb.h to make linux module buildable standalone. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 5632639 - Browse repository at this point
Copy the full SHA 5632639View commit details -
Cast the time type to (long). This is correct on all architectures. On i386, this promotes the int time_t to a long (which is also 32-bit). On 64-bit architectures, this promotes the 64-bit signed time_t to a 64-bit signed int type. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 3edee2f - Browse repository at this point
Copy the full SHA 3edee2fView commit details -
cdev_pager_allocate(): ensure that the cdev_pager_ops ctr is called o…
…nly once per allocated vm_object. Otherwise, since constructors are not idempotent, we e.g. leak device reference in case of non-managed pager. PR: 278826 Reported by: Austin Zhang <[email protected]> Reviewed by: alc, markj Tested by: pho Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45113
Configuration menu - View commit details
-
Copy full SHA for 439743b - Browse repository at this point
Copy the full SHA 439743bView commit details -
Sponsored by: The FreeBSD Foundation MFC after: 1 week
Configuration menu - View commit details
-
Copy full SHA for 470cbb8 - Browse repository at this point
Copy the full SHA 470cbb8View commit details -
linprocfs: Really fix time_t type issue
The cast to (long) is wrong on all the other 32-bit platforms. (long long) is the correct type on all platforms. Also, use a z modifier for size_t which also fails on 32-bit platforms. Fixes: 02f481a Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for b6cf5e4 - Browse repository at this point
Copy the full SHA b6cf5e4View commit details -
ipfw: Fix a typo in a source code comment
- s/defaul/default/ MFC after: 3 days
Configuration menu - View commit details
-
Copy full SHA for 825b225 - Browse repository at this point
Copy the full SHA 825b225View commit details -
Configuration menu - View commit details
-
Copy full SHA for 502c94b - Browse repository at this point
Copy the full SHA 502c94bView commit details -
bsdinstall: Remove unused variables in fetchmissingdists
ALL_DISTRIBUTIONS and VERIFY_MANIFEST_SIG They are neither used in the script nor exported. Not referenced anywhere in bsdinstall/* Approved by: imp@ Differential Revision: https://reviews.freebsd.org/D42369
Configuration menu - View commit details
-
Copy full SHA for 1a3b736 - Browse repository at this point
Copy the full SHA 1a3b736View commit details -
arm64: map kernel using large pages when page size is 16K
When the page size is 16K, use ATTR_CONTIGUOUS to map the kernel code and data sections using 2M pages. Previously, they were mapped using 16K pages. Reviewed by: markj Tested by: markj Differential Revision: https://reviews.freebsd.org/D45162
Configuration menu - View commit details
-
Copy full SHA for b4f5ac5 - Browse repository at this point
Copy the full SHA b4f5ac5View commit details -
Import _FORTIFY_SOURCE implementation from NetBSD
This is a mostly-unmodified copy of the various *_chk implementations and headers from NetBSD, without yet modifying system headers to start actually including them. A future commit will also apply the needed bits to fix ssp/unistd.h. Reviewed by: imp, pauamma_gundo.com (both previous versions), kib Sponsored by: Stormshield Sponsored by: Klara, Inc. Differential Revision: https://reviews.freebsd.org/D32306
Configuration menu - View commit details
-
Copy full SHA for 56f274b - Browse repository at this point
Copy the full SHA 56f274bView commit details -
Prepare the system for _FORTIFY_SOURCE
Notably: - libc needs to #undef some of the macros from ssp/* for underlying implementations - ssp/* wants a __RENAME() macro (snatched more or less from NetBSD) There's some extra hinkiness included for read(), since libc spells it as "_read" while the rest of the world spells it "read." Reviewed by: imp, ngie Sponsored by: Stormshield Sponsored by: Klara, Inc. Differential Revision: https://reviews.freebsd.org/D32307
Configuration menu - View commit details
-
Copy full SHA for fcc658c - Browse repository at this point
Copy the full SHA fcc658cView commit details -
Add a build knob for _FORTIFY_SOURCE
In the future, we will Default to _FORTIFY_SOURCE=2 if SSP is enabled, otherwise default to _FORTIFY_SOURCE=0. For now we default it to 0 unconditionally to ease bisect across older versions without the new symbols, and we'll put out a call for testing. include/*.h include their ssp/*.h equivalents as needed based on the knob. Programs and users are allowed to override FORTIFY_SOURCE in their Makefiles or src.conf/make.conf to force it off. Reviewed by: des, markj Relnotes: yes Sponsored by: Stormshield Sponsored by: Klara, Inc. Differential Revision: https://reviews.freebsd.org/D32308
Configuration menu - View commit details
-
Copy full SHA for 157e6ab - Browse repository at this point
Copy the full SHA 157e6abView commit details -
access.2: Mention that lstat(2) should be used for symbolic links
access(), eaccess() and faccessat() will always dereference symbolic links. So add a note in the manual page, that lstat(2) should be used in the case of symbolic links. PR: 262895 Reviewed by: gbe, pauamma_gundo.com MFC after: 1 week Differential Revision: https://reviews.freebsd.org/D44890
Configuration menu - View commit details
-
Copy full SHA for fcd13aa - Browse repository at this point
Copy the full SHA fcd13aaView commit details -
User misconfiguration may lead to routing loops where we try to send the tunnel packet into the tunnel. This eventually leads to stack overflows and panics. Avoid this using if_tunnel_check_nesting(), which will drop the packet if we're looping or we hit three layers of nested tunnels. MFC after: 1 week Sponsored by: Rubicon Communications, LLC ("Netgate")
Configuration menu - View commit details
-
Copy full SHA for 781415e - Browse repository at this point
Copy the full SHA 781415eView commit details -
expand: Fix markup for the
-t
option.PR: 274897 Fixes: 8993d78 MFC after: 3 days Reviewed by: gbe Differential Revision: https://reviews.freebsd.org/D45167
Configuration menu - View commit details
-
Copy full SHA for 5620b7b - Browse repository at this point
Copy the full SHA 5620b7bView commit details -
syscalls.master: allow vfork(2) in capsicum(4) capability mode
There is no reason not do do this, we already allow fork(2), and I need vfork(2) for CHERI process colocation. Reviewed by: brooks, emaste, oshogbo MFC after: 1 week Differential Revision: https://reviews.freebsd.org/D39829
Configuration menu - View commit details
-
Copy full SHA for 895d2ae - Browse repository at this point
Copy the full SHA 895d2aeView commit details -
src.conf.5: regen after addition of _FORTIFY_SOURCE build knob
Regen to pick up WITHOUT_SSP addition from commit 9bfd3b4. Sponsored by: The FreeBSD Foundation
Configuration menu - View commit details
-
Copy full SHA for 4788eaa - Browse repository at this point
Copy the full SHA 4788eaaView commit details -
Fix the GCC build after _FORTIFY_SOURCE import
We haven't exposed gets(3) in a long time, rip out __gets_chk before it's too late and something builds a gets(3) user with it enabled.
Configuration menu - View commit details
-
Copy full SHA for a9b4027 - Browse repository at this point
Copy the full SHA a9b4027View commit details -
Configuration menu - View commit details
-
Copy full SHA for d80942c - Browse repository at this point
Copy the full SHA d80942cView commit details -
tmpfs: recalculate OBJ_TMPFS_VREF on reinstantiating node' vnode
Reported and tested by: pho Reviewed by: markj Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45119
Configuration menu - View commit details
-
Copy full SHA for dbb8a05 - Browse repository at this point
Copy the full SHA dbb8a05View commit details -
swap-like pagers: assert that writemapping decrease does not pass zero
Reviewed by: markj Tested by: pho Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45119
Configuration menu - View commit details
-
Copy full SHA for 04cea98 - Browse repository at this point
Copy the full SHA 04cea98View commit details -
tmpfs_destroy_vobject(): clear v_object under the object lock
Which allows tmpfs_pager_writecount_recalc() to reliably detect reclaimed vnode and make its accesses to object->un_pager.swp.private (== vp) safe against reclaim. Note that vnode instantiation already assigns v_object under the object lock. Reviewed by: markj Reported and tested by: pho Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45119
Configuration menu - View commit details
-
Copy full SHA for be7cbea - Browse repository at this point
Copy the full SHA be7cbeaView commit details -
Configuration menu - View commit details
-
Copy full SHA for 055d1ac - Browse repository at this point
Copy the full SHA 055d1acView commit details -
nvme: Use strlcpy instead of strncpy to ensure termination
Reviewed by: dab, imp Sponsored by: Chelsio Communications Differential Revision: https://reviews.freebsd.org/D45152
Configuration menu - View commit details
-
Copy full SHA for 0d9aa18 - Browse repository at this point
Copy the full SHA 0d9aa18View commit details -
nvme/f: Use strlcpy instead of strncpy + manual string termination
Reviewed by: dab, imp Sponsored by: Chelsio Communications Differential Revision: https://reviews.freebsd.org/D45153
Configuration menu - View commit details
-
Copy full SHA for 88f2a00 - Browse repository at this point
Copy the full SHA 88f2a00View commit details -
nvme_qpair_complete_tracker and nvme_qpair_manual_complete_tracker have to be called without the qpair lock, so assert its unowned. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 1ff5337 - Browse repository at this point
Copy the full SHA 1ff5337View commit details -
nvme: Slight reworking this loop to match FreeBSD style
Update the comment for the code, and slightly rework the code in the 'fast exit' paradigm that FreeBSD generally tries to do. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 6520dcb - Browse repository at this point
Copy the full SHA 6520dcbView commit details -
We don't need to dereference qpair to get the ctrlr pointer each time, so use the cached value. It's not going to change. No change intended. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 501493d - Browse repository at this point
Copy the full SHA 501493dView commit details -
nvme: Add comment about where tr->deadline is set
It's easy to overlook the chain of events that lead to tr->deadline being updated. Add a comment here to explain what otherwise looks like an oversight w/o careful study. Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 4283010 - Browse repository at this point
Copy the full SHA 4283010View commit details -
include: ssp: kill off leftover $FreeBSD$ tag
Most of these were fixed when rebasing the patch forward, but this one seems to have been missed. Reported by: marck Fixes: be04fec ("Import _FORTIFY_SOURCE implementation [...]")
Configuration menu - View commit details
-
Copy full SHA for a4d5ef9 - Browse repository at this point
Copy the full SHA a4d5ef9View commit details -
These were previously installed by the GCC implementation of libssp, but now they're installed once again with our implementation of FORTIFY_SOURCE. Reported by: jkim Fixes: be04fec ("Import _FORTIFY_SOURCE implementation [...]")
Configuration menu - View commit details
-
Copy full SHA for d5a97db - Browse repository at this point
Copy the full SHA d5a97dbView commit details -
freebsd-tips: Add fortune to find font providing Unicode character
Reviewed by: emaste Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D45183
Configuration menu - View commit details
-
Copy full SHA for 85bd184 - Browse repository at this point
Copy the full SHA 85bd184View commit details -
x86: Add Intel TD/HFI related MSR/CPUID defines to specialregs.h
for the coredirector driver. MFC after: 1 week Differential revision: https://reviews.freebsd.org/D44453
Configuration menu - View commit details
-
Copy full SHA for 06ce4a4 - Browse repository at this point
Copy the full SHA 06ce4a4View commit details -
boottrace: Use NULL for SYSINIT's last arg, which is a pointer type
MFC after: 3 days
Configuration menu - View commit details
-
Copy full SHA for 0702663 - Browse repository at this point
Copy the full SHA 0702663View commit details -
arm64_pmap: narrow scope of bti_same test
The pmap_bti_same test in pmap_enter_l3c only happens in the !ADDR_IS_KERNEL case; in the other case, a KASSERT fails. So move the test into that case to save a bit of time when ADDR_IS_KERNEL. Reviewed by: andrew Differential Revision: https://reviews.freebsd.org/D45160
Configuration menu - View commit details
-
Copy full SHA for 32bfc5e - Browse repository at this point
Copy the full SHA 32bfc5eView commit details -
Merge commit '3c2ab5fddc576e58f3ffa70dc5fa95144646a513'
Configuration menu - View commit details
-
Copy full SHA for 8c83df2 - Browse repository at this point
Copy the full SHA 8c83df2View commit details -
ifconfig: Add format shortcuts.
MFC after: 1 week Reviewed by: imp Differential Revision: https://reviews.freebsd.org/D45166
Configuration menu - View commit details
-
Copy full SHA for 7ab3e16 - Browse repository at this point
Copy the full SHA 7ab3e16View commit details -
nuageinit: by default to not enable nuageinit
MFC After: 1 day Reported by: karels@
Configuration menu - View commit details
-
Copy full SHA for 4ec4245 - Browse repository at this point
Copy the full SHA 4ec4245View commit details -
Configuration menu - View commit details
-
Copy full SHA for 3d02680 - Browse repository at this point
Copy the full SHA 3d02680View commit details -
Configuration menu - View commit details
-
Copy full SHA for 84ca971 - Browse repository at this point
Copy the full SHA 84ca971View commit details -
snd_hda: Add patch for Lenovo Ideapad 3
Reported by: [email protected] Sponsored by: The FreeBSD Foundation MFC after: 3 days Reviewed by: emaste Differential Revision: https://reviews.freebsd.org/D45100
Configuration menu - View commit details
-
Copy full SHA for 400adfc - Browse repository at this point
Copy the full SHA 400adfcView commit details -
snd_hda: Rename LENOVO_I* to LENOVO_IDEAPAD*
Sponsored by: The FreeBSD Foundation MFC after: 3 days Reviewed by: emaste Differential Revision: https://reviews.freebsd.org/D45105
Configuration menu - View commit details
-
Copy full SHA for 6d63351 - Browse repository at this point
Copy the full SHA 6d63351View commit details -
sound: Remove ncards variable from sound_oss_card_info()
The loop counter is also the card's index, so ncards is redundant. Sponsored by: The FreeBSD Foundation MFC after: 3 days Reviewed by: dev_submerge.ch Differential Revision: https://reviews.freebsd.org/D45144
Configuration menu - View commit details
-
Copy full SHA for 2c67e6c - Browse repository at this point
Copy the full SHA 2c67e6cView commit details -
awk: Merge in bsd-feature branch of OTA from 20240422 (31bb33a32f71)
In the last 2nd edition import, I mistakenly grabbed from the 'main' branch of upstream rather than the bsd-feature branch. This means that we have a regression in awk from that point forward: all the BSD-specific bit functions (and a few others) were dropped. This restores it at the same level. MFC After: 1 day Sponsored by: Netflix
Configuration menu - View commit details
-
Copy full SHA for 05c751a - Browse repository at this point
Copy the full SHA 05c751aView commit details -
net80211: add the 802.11-2016 cipher list to the crypto array set.
These are the bitmap / cipher module number fields used for net80211 ciphers. This requires a kernel recompile, but nothing (currently) in userland is using these. Differential Revision: https://reviews.freebsd.org/D44899 Reviewed by: bz, cc
Configuration menu - View commit details
-
Copy full SHA for 6542258 - Browse repository at this point
Copy the full SHA 6542258View commit details -
net80211: add placeholder module names for the new ciphers
This is effectively a no-op as we currently don't advertise these ciphers as available anywhere. Note though the intent to support 128 and 256 bit ciphers in the same crypto module. Differential Revision: https://reviews.freebsd.org/D44900 Reviewed by: cc, cy Approved by: cc, cy
Configuration menu - View commit details
-
Copy full SHA for 2a94f9d - Browse repository at this point
Copy the full SHA 2a94f9dView commit details -
net80211: allow a single wlan crypto module to register for >1 cipher
This allows a single wlan crypto module to register for more than one cipher. Without it, duplicate linkerset structs are initialised for the actual module loading machinery itself. I've tested this in my private tree with wlan_ccmp providing both 128 and 256 bit cipher support. Differential Revision: https://reviews.freebsd.org/D44901 Reviewed by: bz, cc, cy Approved by: bz, cc, cy
Configuration menu - View commit details
-
Copy full SHA for 4ddc12a - Browse repository at this point
Copy the full SHA 4ddc12aView commit details -
net80211: add initial key management suites from 802.11-2016, APIs to…
… register them The WPA1/WPA2 driver capabilities aren't really enough in today's world. There are a /lot/ more key management suites to support! So, add initial support for net80211 and drivers to announce what key management suites are supported. These are the list from 802.11-2016 section 9.4.2.25.3 (AKM suites.) The flags are for software supported key management. Drivers may support more key management suites and are welcome to announce more; net80211 will only announce ones that we know net80211 knows "enough" about to support correctly. There /are/ other suites that may be interesting to some people in the future that are not part of this set - eg if anyone ever wants to support the Chinese WAPI standard - so this bitmap is not specifically just the AKM suites in the RSN OUI. This should eventually be communicated up to the wpa_supplicant and hostapd via a replacement driver/vap capabilities call so they know what to enable rather than just IEEE80211_C_WPA1 / IEEE80211_C_WPA2. Differential Revision: https://reviews.freebsd.org/D44919 Reviewed by: bz
Configuration menu - View commit details
-
Copy full SHA for 7bd095c - Browse repository at this point
Copy the full SHA 7bd095cView commit details -
AMD CPUs: update bits and data from CPUID 0x8000_0008
from AMD APM vol3 doc no 24594 Rev. 3.36 March 2024 Reviewed and tested by: emaste Sponsored by: Advanced Micro Devices (AMD) Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45188
Configuration menu - View commit details
-
Copy full SHA for 0fdace6 - Browse repository at this point
Copy the full SHA 0fdace6View commit details -
ssp: appease -Wgnu-statement-expression-from-macro-expansion
It's a stupid warning, but some ports enable it by default and were already defining _FORTIFY_SOURCE, thus exposing the new macros immediately. This at least fixes the libfido2 build, perhaps others as well. While we're here, fix a fresh build of stand w/ FORTIFY_SOURCE enabled by not pulling in the ssp headers if _STANDALONE is defined. We do not have runtime support in libsa as of the time of writing. Reported by: netchild Sponsored by: Stormshield Sponsored by: Klara, Inc.
Configuration menu - View commit details
-
Copy full SHA for 0522acf - Browse repository at this point
Copy the full SHA 0522acfView commit details -
Enable soft updates by default for UFS2 filesystems.
Soft updates dramatically improve the performance of UFS filesystems. The newfs(8) utility currently does not enable them by default. The FreeBSD installer enables soft updates by default. However custom built installations that do not specify the -U option to newfs(8) and the prebuilt UFS system images get filesystems without soft updates enabled. There are several testing sites that run benchmarks comparing the performance of Linux distributions versus BSD distributions. When they run filesystem comparison benchmarks they use newfs(8) to create the UFS filesystem. Because it does not have soft updates enabled it runs poorly versus the Linux ext4 filesystem. When I have suggested to them that they should enable soft updates on the UFS filesystem in their testing their response is that they expect the utility that creates the filesystem to use optimal defaults and that they cannot be expected to fiddle with various option settings. The purpose of this change is to give a filesystem created with newfs(8) reasonably optimal settings. For UFS2 this means enabling soft updates. For UFS1 which tends to be used on small systems with minimal memory and CPU speed, the lower memory footprint of running without soft updates is a more sensible default. This change adds a note in the section of the newfs(8) manual page that describes the -U option for enabling soft updates that they are enabled by default for UFS2 filesystems and that they can be disabled by using tunefs(8). Reviewed-by: Warner Losh, kib MFC after: 1 week Differential Revision: https://reviews.freebsd.org/D45201
Configuration menu - View commit details
-
Copy full SHA for 6a7c3c3 - Browse repository at this point
Copy the full SHA 6a7c3c3View commit details -
Issue CTSRD-CHERI#237 : Resolver uses nameserver commented out in /et…
…c/resolv.conf This /etc/resolv.conf: # x # nameserver 8.8.8.8 Still configured 8.8.8.8 as nameserver, because the comment detection in `ldns_resolver_new_frm_fp_l()` didn't anticipate empty lines before the comment. This fix removed all comment handling from `ldns_resolver_new_frm_fp_l()`. Instead a new function is introduced `ldns_fget_token_l_resolv_conf()` that skips comments that start with '#' and ';'. The old `ldns_fget_token_l()` (that is used for zonefiles too) still accepts only ';' for comments.
Configuration menu - View commit details
-
Copy full SHA for 60591bb - Browse repository at this point
Copy the full SHA 60591bbView commit details -
atf: Guard against multiple evaluation.
Note that the ATF-C++ macros have the same issue, but they are not as easily fixed. MFC after: 3 days Reviewed by: ngie Differential Revision: https://reviews.freebsd.org/D45148
Configuration menu - View commit details
-
Copy full SHA for ec4b5a1 - Browse repository at this point
Copy the full SHA ec4b5a1View commit details -
Revert "Issue CTSRD-CHERI#237 : Resolver uses nameserver commented ou…
…t in /etc/resolv.conf" This reverts commit b5fb1f4.
Configuration menu - View commit details
-
Copy full SHA for f788ff8 - Browse repository at this point
Copy the full SHA f788ff8View commit details -
ldns: Ignore commented-out lines in resolv.conf.
This merges upstream PR 238 + an additional bug fix. PR: 278721 MFC after: 1 week
Configuration menu - View commit details
-
Copy full SHA for ff4132b - Browse repository at this point
Copy the full SHA ff4132bView commit details -
adduser: Additional variable fixes.
One function used `_input` without making it local, causing its value to leak into other functions. This broke the `-f` case. Fix that instance and initialize all local variables that weren't already initialized. Fixes: 170d088 MFC after: 3 days Reviewed by: karels Differential Revision: https://reviews.freebsd.org/D45204
Configuration menu - View commit details
-
Copy full SHA for 7169833 - Browse repository at this point
Copy the full SHA 7169833View commit details -
MFC after: 3 days Reviewed by: imp, allanjude Differential Revision: https://reviews.freebsd.org/D45209
Configuration menu - View commit details
-
Copy full SHA for 01471b2 - Browse repository at this point
Copy the full SHA 01471b2View commit details -
freebsd-tips: Tweak fortune to find font providing Unicode character
While here, remove my name and email address. Reported by: bapt Sponsored by: The FreeBSD Foundation
Configuration menu - View commit details
-
Copy full SHA for 68f2c62 - Browse repository at this point
Copy the full SHA 68f2c62View commit details -
uart: Honour clock-frequency in FDT for UART_FDT_CLASS if present
The StarFive VisionFive 2 has a Synopsys DesignWare ABP UART, whose driver uses UART_FDT_CLASS rather than UART_FDT_CLASS_AND_DEVICE as it has its own separate newbus driver. This UART is driven by a 24MHz clock as specified in the FDT, but we don't currently look at the property here, instead passing down 0 and letting the default value be used in the 8250 driver (~1.8MHz). As a result the divisor is misconfigured for the current baud rate for the entire kernel boot process. Once the newbus driver attaches the correct frequency is saved in the softc, but that does not take effect until the next time ns8250_param is called and the divisor is recalculated, namely when userspace runs and /dev/console is opened (note that ns8250_init does not get called when the newbus device corresponding to the current console attaches). Fix this issue by attemmpting to get the current clock frequency as for the UART_FDT_CLASS_AND_DEVICE_CASE, but falling back to 0 rather than failing on error. Reviewed by: imp, mhorne Differential Revision: https://reviews.freebsd.org/D45159
Configuration menu - View commit details
-
Copy full SHA for b365718 - Browse repository at this point
Copy the full SHA b365718View commit details -
riscv: fix L0 PTE setup (Sv48)
Per the Privilege Spec, the Accessed (A) or Dirty (D) bits must only be set for a leaf PTE. It seems newer versions of QEMU have started to enforce this requirement, and without this change, pmap_bootstrap() hangs when switching to Sv48 mode. Reviewed by: jrtc27, markj MFC after: 3 days Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D45210
Configuration menu - View commit details
-
Copy full SHA for 70338b9 - Browse repository at this point
Copy the full SHA 70338b9View commit details -
vfs_domount_update(): style, use space instead of tab
Noted by: mckusick Sponsored by: The FreeBSD Foundation MFC after: 3 days
Configuration menu - View commit details
-
Copy full SHA for bbb08bd - Browse repository at this point
Copy the full SHA bbb08bdView commit details -
vfs_domount_update(): postpone setting MNT_UNION until VFS_MOUNT() is…
… done The file system that handles updating the mount point might do lookups during the update, in which case it could find the flag MNT_UNION set on the mp while mount point is still not updated. In particular, the rootvp->v_mount->mnt_vnodecovered is not yet set. Delay setting MNT_UNION until the mount is performed. PR: 265311 Reported by: Robert Morris <[email protected]> Reviewed by: mckusick, olce Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45208
Configuration menu - View commit details
-
Copy full SHA for 244516e - Browse repository at this point
Copy the full SHA 244516eView commit details -
linuxkpi: spinlock: Simplify code
Just use a typedef for spinlock_t, no need to create a useless structure. Reviewed by: bz, emaste Sponsored by: Beckhoff Automation GmbH & Co. KG Differential Revision: https://reviews.freebsd.org/D45205
Configuration menu - View commit details
-
Copy full SHA for 91c6ed6 - Browse repository at this point
Copy the full SHA 91c6ed6View commit details -
linuxkpi: rwlock: Simplify code
Just use a typedef for rwlock_t, no need to create a useless structure. Reviewed by: bz Sponsored by: Beckhoff Automation GmbH & Co. KG Differential Revision: https://reviews.freebsd.org/D45206
Configuration menu - View commit details
-
Copy full SHA for 3f3a501 - Browse repository at this point
Copy the full SHA 3f3a501View commit details -
linuxkpi: refcount: Use atomic_t directly
Simply use a typedef for refcount_t on atomic_t, this allow us to use a nativ type and also changing struct kref to directly use a refcount_t like Linux. Reviewed by: bz Sponsored by: Beckhoff Automation GmbH & Co. KG Differential Revision: https://reviews.freebsd.org/D45207
Configuration menu - View commit details
-
Copy full SHA for 132245a - Browse repository at this point
Copy the full SHA 132245aView commit details -
contrib/bsddialog: Import version 1.0.2
Implicitly import also 1.0.1, both versions are for fixing and feature requests. Fixing: Change --mixedform behavior to fix a bsdinstall fault avoiding to change the command line in wlanconfig. Feature requests: * Add keys to navigate menus. * Add key to redraw dialogs. * Avoid to handle env NCURSES_NO_UTF8_ACS in PuTTY. See '2024-04-11 Version 1.0.2' and '2023-11-16 Version 1.0.1' in /usr/src/contrib/bsddialog/CHANGELOG for more detailed information. PR: 274472 Differential Revision: D42380 Merge commit 'be8846bd9e069f4a6bea3d769005bea96cf43990'
Configuration menu - View commit details
-
Copy full SHA for c67ffbb - Browse repository at this point
Copy the full SHA c67ffbbView commit details -
man filesystems: move driver pages to section four
Filesystem manual pages describe drivers, not formats; except for fs, which describes the structures of ffs/ufs, not how to use it in the system. Reported by: emaste Reviewed by: des, imp, meena (previous version) Pull Request: freebsd/freebsd-src#1077
Configuration menu - View commit details
-
Copy full SHA for 331b6e2 - Browse repository at this point
Copy the full SHA 331b6e2View commit details -
man filesystems: ObsoleteFiles after move to sec 4
Reported by: imp Reviewed by: des, imp Pull Request: freebsd/freebsd-src#1077
Configuration menu - View commit details
-
Copy full SHA for 96a01c6 - Browse repository at this point
Copy the full SHA 96a01c6View commit details -
man filesystems: fix xrefs after move to section 4
Reviewed by: des, imp Pull Request: freebsd/freebsd-src#1077
Configuration menu - View commit details
-
Copy full SHA for 748984b - Browse repository at this point
Copy the full SHA 748984bView commit details -
netstat(1): increase width of Netif column
The previous width of Netif (10 or 8) was too short for modern interface names; make it 12, which is long enough to display "epair0a.1000". This came up in practice with genet(4) interfaces, since the base interface name is long enough that with the previous limit, VLAN identifiers would be truncated at 1 character in the IPv6 output: "genet0.100" becomes "genet0.1". The width is now fixed, and doesn't depend on the address family, because there's no reason that length of the interface name would vary based on the AF. Reviewed by: imp,zlei,Mina Galić Pull Request: freebsd/freebsd-src#1223
Configuration menu - View commit details
-
Copy full SHA for ca39109 - Browse repository at this point
Copy the full SHA ca39109View commit details -
netstat(8): for -W, use IFNAMSIZ
If -W is specified, use IFNAMSIZ as the width of the Netif column, instead of the default 12. Reviewed by: imp,zlei,Mina Galić Pull Request: freebsd/freebsd-src#1223
Configuration menu - View commit details
-
Copy full SHA for 0d413bd - Browse repository at this point
Copy the full SHA 0d413bdView commit details -
sys/modules/dpdk_lpm4: do not build without INET
Reviewed by: imp Pull Request: freebsd/freebsd-src#1236
Configuration menu - View commit details
-
Copy full SHA for 92fa3ce - Browse repository at this point
Copy the full SHA 92fa3ceView commit details -
In bhyve_parse_config_option(), a string is allocated and passed to nvlist_add_string() but not free'd afterwards. Reported by: Coverity CID: 1544049 Sponsored by: The FreeBSD Foundation Reviewed by: imp Pull Request: freebsd/freebsd-src#1234
Configuration menu - View commit details
-
Copy full SHA for e70dc14 - Browse repository at this point
Copy the full SHA e70dc14View commit details -
The str variable in cctl_nvlist_end_element() does not get free()'d when converted to an integer value. (name is "trtype") Reported by: Coverity Scan Coverity ID: 1545039 Sponsored by: The FreeBSD Foundation Reviewed by: imp Pull Request: freebsd/freebsd-src#1237
Configuration menu - View commit details
-
Copy full SHA for d293b2e - Browse repository at this point
Copy the full SHA d293b2eView commit details -
makeman: extend duplicate option warning to OPT_ options
In a local tree I accidentally had OPT_INIT_ALL defaulting to zero in userland and none in kernel. This resulted in the INIT_ALL text appearing twice in src.conf.5. Reviewed by: brooks Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D45184
Configuration menu - View commit details
-
Copy full SHA for e6f43b3 - Browse repository at this point
Copy the full SHA e6f43b3View commit details -
linuxkpi: Provide a non-NULL value for THIS_MODULE
THIS_MODULE is used to differentiate modules on Linux. We currently completely stub out any Linux struct module usage, but THIS_MODULE is still used to populate the "owner" fields of various drivers. Even though we don't actually dereference these "owner" fields they are still used by drivers to check if devices/dmabufs/etc come from different modules. For example, during DRM GEM import some drivers check if the dmabuf's owner matches the dev's owner. If they match because they are both NULL drivers may incorrectly think two resources come from the same module. This adds a general purpose __this_linker_file which will point to the linker file of the module that uses it. We can then use that pointer to have a valid value for THIS_MODULE. Reviewed by: bz, jhb Differential Revision: https://reviews.freebsd.org/D44306
Configuration menu - View commit details
-
Copy full SHA for 964958f - Browse repository at this point
Copy the full SHA 964958fView commit details -
SysV SHM: move SHMSEG constants to sys/shm.h
There are planned consumers in linprocfs. Tested by: Ricardo Branco <[email protected]> Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45175
Configuration menu - View commit details
-
Copy full SHA for 2e8f4a2 - Browse repository at this point
Copy the full SHA 2e8f4a2View commit details -
SysV IPC: provide in-kernel helpers to obtain ipcs(8)-like information
PR: 278949 Reviewed by: markj Tested by: Ricardo Branco <[email protected]> Sponsored by: The FreeBSD Foundation MFC after: 1 week Differential revision: https://reviews.freebsd.org/D45175
Configuration menu - View commit details
-
Copy full SHA for 909f960 - Browse repository at this point
Copy the full SHA 909f960View commit details -
libcapsicum: document return values
Reviewed by: emaste Requested by: des Differential Revision: https://reviews.freebsd.org/D45222
Configuration menu - View commit details
-
Copy full SHA for 6a65b72 - Browse repository at this point
Copy the full SHA 6a65b72View commit details -
Merge commit 87f3407856e6 from llvm-project (by Phoebe Wang):
[X86][Driver] Do not add `-evex512` for `-march=native` when the target doesn't support AVX512 (#91694) This prevents problems with ports that fail to build with CPUTYPE=native, if the native CPU supports AVX512F, resulting in errors like: /wrkdirs/usr/ports/archivers/libdeflate/work/libdeflate-1.20/lib/x86/adler32_template.h:197:21: error: always_inline function '_mm512_set1_epi8' requires target feature 'evex512', but would be inlined into function 'adler32_x86_avx512_vl512_vnni' that is compiled without support for 'evex512' 197 | const vec_t ones = VSET1_8(1); | ^ /wrkdirs/usr/ports/archivers/libdeflate/work/libdeflate-1.20/lib/x86/adler32_template.h:116:23: note: expanded from macro 'VSET1_8' 116 | # define VSET1_8(a) _mm512_set1_epi8(a) | ^ /wrkdirs/usr/ports/archivers/libdeflate/work/libdeflate-1.20/lib/x86/adler32_template.h:197:21: error: AVX vector return of type '__m512i' (vector of 8 'long long' values) without 'evex512' enabled changes the ABI /wrkdirs/usr/ports/archivers/libdeflate/work/libdeflate-1.20/lib/x86/adler32_template.h:116:23: note: expanded from macro 'VSET1_8' 116 | # define VSET1_8(a) _mm512_set1_epi8(a) | ^ Ports known to be affected are: archivers/libdeflate, devel/highway, www/node20, and lang/rust. (For rust itself there is also a similar issue reported at rust-lang/rust#121088). PR: 276104 Reported by: netchild MFC after: 3 days
Configuration menu - View commit details
-
Copy full SHA for 6432473 - Browse repository at this point
Copy the full SHA 6432473View commit details -
Trim a spurious trailing backslash
Reported by: dim Fixes: 1687d77 man filesystems: move driver pages to section four
Configuration menu - View commit details
-
Copy full SHA for c660606 - Browse repository at this point
Copy the full SHA c660606View commit details -
Some linux code re-init some spinlock so add MTX_NEW to mtx_init. Reported by: David Wolfskill <[email protected]> Fixes: ae38a1a ("linuxkpi: spinlock: Simplify code")
Configuration menu - View commit details
-
Copy full SHA for 0ab456b - Browse repository at this point
Copy the full SHA 0ab456bView commit details -
linuxkpi: rwlock: Fix rwlock_init
Some linux code re-init some spinlock so add MTX_NEW to mtx_init. Reported by: rlibby Fixes: 5c0a192 ("linuxkpi: rwlock: Simplify code")
Configuration menu - View commit details
-
Copy full SHA for 41e5eed - Browse repository at this point
Copy the full SHA 41e5eedView commit details -
rtld: Add MD_OBJ_ENTRY to extend Struct_Obj_Entry
Add a macro the architectures can use to add per-arch fields to Struct_Obj_Entry. Reviewed by: kib Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45116
Configuration menu - View commit details
-
Copy full SHA for 84e55e6 - Browse repository at this point
Copy the full SHA 84e55e6View commit details -
This will be used to handle the DT_AARCH64_VARIANT_PCS tag. Reviewed by: kib Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45117
Configuration menu - View commit details
-
Copy full SHA for 686f3e9 - Browse repository at this point
Copy the full SHA 686f3e9View commit details -
rtld: Add support for arm64 variant pcs
The aarch64 ELF spec has support for a variant of the normal procedure call standard that doesn't follow the normal register convention, e.g. using more registers as arguments, or different register state is preserved. Add support to rtld to handle this. As we don't know which registers need to be preserved disable lazy binding for these functions. Reviewed by: kib Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D44869
Configuration menu - View commit details
-
Copy full SHA for e047efe - Browse repository at this point
Copy the full SHA e047efeView commit details -
rtld: Add arm64 variant pcs tests
When marking a function as variant pcs we can use registers not normally used in procedure calls. Add a test that uses this and stores all general purpose registers to a buffer and compare this buffer with the expected value later. Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D44870
Configuration menu - View commit details
-
Copy full SHA for 336a7cd - Browse repository at this point
Copy the full SHA 336a7cdView commit details -
rtld: Move powerpc specific code to powerpc files
There are two variables set by dynamic tags in the powerpc runtime linker. Now we have a way to split out architecture-specific dynamic tags use it to handle these. Reviewed by: kib, jhibbits Obtained from: jhibbits (earlier version) Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45182
Configuration menu - View commit details
-
Copy full SHA for 9ce9e14 - Browse repository at this point
Copy the full SHA 9ce9e14View commit details -
arm64: Add MRS_REG_ALT_NAME ID register macros
These can be used even when the compiler is too old for the register to be included. Reviewed by: Zachary Leaf <[email protected]> Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45176
Configuration menu - View commit details
-
Copy full SHA for 1a52430 - Browse repository at this point
Copy the full SHA 1a52430View commit details -
arm64: Use the _REG macros to read ID registers
To build with old toolchains use the *_REG macros to access the ID registers. These become a name in the form S?_?_C?_C?_? where the '?' values encode the op and CR values needed to access the register. For consistency use these macros for all ID registers, even if most toolchains understand them. Reviewed by: Zachary Leaf <[email protected]> Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45177
Configuration menu - View commit details
-
Copy full SHA for 6597cc4 - Browse repository at this point
Copy the full SHA 6597cc4View commit details -
Revert "rtld: Add arm64 variant pcs tests"
It's missing an mtree update This reverts commit 9e48c30.
Configuration menu - View commit details
-
Copy full SHA for 7cbe244 - Browse repository at this point
Copy the full SHA 7cbe244View commit details -
tpm: Add new tpm_bus.c to module Makefile
Reported by: eduardo@ Fixes: c2e9c5b ("tpm: Refactor TIS and add a SPI attachment")
Configuration menu - View commit details
-
Copy full SHA for fe2e266 - Browse repository at this point
Copy the full SHA fe2e266View commit details -
arm64/vmm: Fix the build with GCC
- Fix the spelling of handle_el2_el1_irq64 - Add .section before .rodata as the GCC build needs it Sponsored by: Arm Ltd
Configuration menu - View commit details
-
Copy full SHA for 49b145d - Browse repository at this point
Copy the full SHA 49b145dView commit details -
dd a missing underscore to arm_smccc_1_2_* to fix the GCC build. Sponsored by: Arm Ltd
Configuration menu - View commit details
-
Copy full SHA for 22dd1f5 - Browse repository at this point
Copy the full SHA 22dd1f5View commit details -
arm64: make SPE regs use ALT_NAME macro
When the register is not defined in Armv8.0 i.e. added in a later extension, like SPE added in v8.2, the alternative name format of: S<op0>_<op1>_C<crn>_C<crm>_<op2> should be used; otherwise, calls to {READ,WRITE}_SPECIALREG() will fail. Use the MRS_REG_ALT_NAME() macro for SPE changing hex to decimal as required by the macro. Reviewed by: andrew Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45171
Configuration menu - View commit details
-
Copy full SHA for 52ac838 - Browse repository at this point
Copy the full SHA 52ac838View commit details -
arm64: add PMBSR_MSS_{BSC,FSC} status code field
Bits [5:0] of PMBSR_MSS encodes either Buffer Status Code (BSC) or Fault Status Code (FSC) depending on PMBSR_EC value. Add PMBSR_MSS_{BSC,FSC} to cover this field. Reviewed by: andrew Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45172
Configuration menu - View commit details
-
Copy full SHA for ffbd966 - Browse repository at this point
Copy the full SHA ffbd966View commit details -
CONTEXTIDR_EL1 is used in debug and trace features to identify the current process or context. Reviewed by: andrew Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45173
Configuration menu - View commit details
-
Copy full SHA for 5a029b0 - Browse repository at this point
Copy the full SHA 5a029b0View commit details -
aarch64: disable LIB32 with gcc
gcc doesn't have -m32 support on aarch64 so mark LIB32 broken there. We have to check both COMPILER_TYPE and X_COMPILER_TYPE becuase X_COMPILER_TYPE is only conditionally set and COMPILER_TYPE is the host compiler in Makefile.inc1. Reviewed by: emaste Differential Revision: https://reviews.freebsd.org/D45089
Configuration menu - View commit details
-
Copy full SHA for 1fe4168 - Browse repository at this point
Copy the full SHA 1fe4168View commit details -
Since at least 2022 (see https://reviews.freebsd.org/D36754), it has not been possible to build armv6/armv7 with gcc due to atomics macros gcc doesn't like. Prevent developers doing due diligance from wasting time and CPU cycles on this combination as it just fails to build in libc. Reviewed by: imp, andrew Differential Revision: https://reviews.freebsd.org/D45193
Configuration menu - View commit details
-
Copy full SHA for 205a1e0 - Browse repository at this point
Copy the full SHA 205a1e0View commit details -
zfs: Avoid a gcc -Wint-to-pointer-cast warning
On 32-bit platforms long long is generally 64-bits. Sufficiently modern versions of gcc (13 in my testing) complains when casting a pointer to an integer of a different width so cast to uintptr_t first to avoid the warning. Fix i386 gcc builds while we wait for this to be merged to OpenZFS. Sponsored by: DARPA, AFRL Pull Request: openzfs/zfs#16203
Configuration menu - View commit details
-
Copy full SHA for 152b622 - Browse repository at this point
Copy the full SHA 152b622View commit details -
uart: DBG2 support to find the debug uart
The Debug Port Table 2 (DBG2) contains information on which devices can be used for debugging purposes. Add support to the uart driver to use the DBG2 table when enabled from loader. Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D44359
Configuration menu - View commit details
-
Copy full SHA for c19bd89 - Browse repository at this point
Copy the full SHA c19bd89View commit details -
arm: Add a missing interrupt to the generic timer
The ACPI generic timer attachment added 3 interrupts, but missed the hypervisor physical interrupt. As the field is present in all versions of the GTDT ACPI table and isn't an optional interrupts we can add it to the interrupts provided to the driver. Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D43974
Configuration menu - View commit details
-
Copy full SHA for a3d3b27 - Browse repository at this point
Copy the full SHA a3d3b27View commit details -
arm: Use the correct irq when in the hypervisor
When booting in the hypervisor state we need to use the hypervisor interrupt in the generic timer. In this case the registers we access in the kernel are remapped to the EL2 versions, however this causes an unexpected interrupt to trigger. Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D43975
Configuration menu - View commit details
-
Copy full SHA for f0d6110 - Browse repository at this point
Copy the full SHA f0d6110View commit details -
arm64: Support break and watch points in VHE
When booting the kernel with VHE it will be running at EL2. The current config register values only enable the reaces at EL1 when tracing the kernel. Set the HMC flag to also trap from EL2. Sponsored by: Arm Ltd Differential Revision: https://reviews.freebsd.org/D45121
Configuration menu - View commit details
-
Copy full SHA for c848377 - Browse repository at this point
Copy the full SHA c848377View commit details -
fib_dxr: check if cached fib_data matches the new request in dxr_init()
When calling dxr_init(), the FIB_ALGO infrastructure may provide a pointer to a previous dxr instance, which permits reuse of auxiliary dxr structures, i.e. incremental lookup structure updates. For dxr this is a crucial feature provided by FIB_ALGO, since dxr incremental updates are typically several orders of magnitude faster than full lookup table rebuilds. However, the auxiliary dxr structure caches a pointer to struct fib_data and relies upon it for performing incremental updates. Apparently, incremental rebuild requests from FIB_ALGO, i.e. a calls to dxr_init() with a pointer old_data set, may (under not yet fully understood circumstances) be invoked within a different fib_data context than the one cached in the previous version of dxr auxiliary structures. In such (rare) events, we ignore the offered old dxr context, and proceed with a full lookup structure rebuild instead of attempting an incremental one using a fib_data context which may or may not no longer be valid, and thus lead to a system crash. PR: 278422 MFC after: 1 week
Configuration menu - View commit details
-
Copy full SHA for c7ffc50 - Browse repository at this point
Copy the full SHA c7ffc50View commit details -
bhyve: avoid resource leak in error path
In e820_finalize(), the e820_fwcfg_item variable, containing the etc/e820 file (for the e820 table from the BIOS) is not free()'d when it could not be added to the QEMU firmware configuration device (fw_cfg). Reported by: Coverity Scan CID: 1522761 Reviewed by: corvink, jhb Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D45223
Configuration menu - View commit details
-
Copy full SHA for ce46c07 - Browse repository at this point
Copy the full SHA ce46c07View commit details -
fib_dxr: do not leak memory if FIB constellation hits structural limit
DXR lookup table encoding has an inherent structural limit on the amount of binary search ranges it can accomodate. With the current IPv4 BGP views (circa 1 M prefixes) and default DXR encoding we are only at around 5% of that limit, so far, far away from hitting it. Just in case it ever gets hit, make sure we free the allocated structures, instead of leaking it. MFC after: 1 week
Configuration menu - View commit details
-
Copy full SHA for 8656600 - Browse repository at this point
Copy the full SHA 8656600View commit details -
fib_dxr: code hygiene, prune old code, no functional changes
The !DXR2 code corresponds to the original DXR encoding proposal from 2012 with a single direct-lookup stage, which is inferior to the more recent (DXR2) variant with two-stage trie both in terms of memory footprint of the lookup structures, and in terms of overall lookup througput. I'm axing the old code chunks to (hopefully) somewhat improve readability, as well as to simplify future maintenance and updates. MFC after: 1 week
Configuration menu - View commit details
-
Copy full SHA for 7fcb90e - Browse repository at this point
Copy the full SHA 7fcb90eView commit details -
libgcc_s: fix nonsense defines
These symbols are present on amd64 or i386. Reported by: kaktus, jhibbits Fixes: 98c8caa libgcc_s: 80-bit long double function are x86-only
Configuration menu - View commit details
-
Copy full SHA for a23b53e - Browse repository at this point
Copy the full SHA a23b53eView commit details -
bhyve: avoid side effect in assertion
An assert() was setting the error variable instead of checking it. Reported by: Coverity Scan CID: 1521431 Reviewed by: jhb Sponsored by: The FreeBSD Foundation Pull Request: freebsd/freebsd-src#1244
Configuration menu - View commit details
-
Copy full SHA for 299662b - Browse repository at this point
Copy the full SHA 299662bView commit details -
libcxxrt: allow build with gcc13 and --no-undefined-version
GCC 13 supports _Float16 and __int128 on fewer architectures than clang and thus libcxxrt compiled with gcc13 is sometimes missing related symbols. Hack around this by explicitly appending --undefined-version to LDFLAGS in problematic cases. Reviewed by: theraven, dim Differential Revision: https://reviews.freebsd.org/D45233
Configuration menu - View commit details
-
Copy full SHA for 30fc36a - Browse repository at this point
Copy the full SHA 30fc36aView commit details -
Mark powerpc* and riscv broken. Refactor and add a TRY_GCC_BROKEN option to build anyway. This simplifies things for people trying to get gcc builds working while letting other developers know that they aren't expected to work. Reviewed by: jhb, emaste Improves: 4c0dfd5 arm: fail early on gcc builds Differential Revision: https://reviews.freebsd.org/D45230
Configuration menu - View commit details
-
Copy full SHA for aae7014 - Browse repository at this point
Copy the full SHA aae7014View commit details -
cxgbe(4): sc->port is indexed by port_id and not tx_chan.
MFC after: 1 week Sponsored by: Chelsio Communications
Configuration menu - View commit details
-
Copy full SHA for e0cef9c - Browse repository at this point
Copy the full SHA e0cef9cView commit details -
cxgbe(4): Consolidate all mk_set_tcb_field_ulp in one place.
MFC after: 1 week Sponsored by: Chelsio Communications
Configuration menu - View commit details
-
Copy full SHA for 93d8ed0 - Browse repository at this point
Copy the full SHA 93d8ed0View commit details -
PR: 278988 Reviewed by: bapt Sponsored by: The FreeBSD Foundation Differential Revision: https://reviews.freebsd.org/D45220
Configuration menu - View commit details
-
Copy full SHA for b1bce6e - Browse repository at this point
Copy the full SHA b1bce6eView commit details