LLVM/project a80d432llvm/lib/Transforms/InstCombine InstCombineSimplifyDemanded.cpp, llvm/test/Transforms/InstCombine simplify-demanded-fpclass.ll

InstCombine: Apply parameter nofpclass in SimplifyDemandedFPClass (#176104)

Apply the use operand's nofpclass to the demanded mask.
DeltaFile
+11-0llvm/test/Transforms/InstCombine/simplify-demanded-fpclass.ll
+5-0llvm/lib/Transforms/InstCombine/InstCombineSimplifyDemanded.cpp
+16-02 files

LLVM/project b1b8410llvm/include/llvm/Support KnownFPClass.h, llvm/lib/Transforms/InstCombine InstCombineSimplifyDemanded.cpp

InstCombine: Handle multiple use copysign

Handle multiple use copysign in SimplifyDemandedFPClass
DeltaFile
+36-3llvm/lib/Transforms/InstCombine/InstCombineSimplifyDemanded.cpp
+7-7llvm/test/Transforms/InstCombine/simplify-demanded-fpclass.ll
+7-0llvm/include/llvm/Support/KnownFPClass.h
+50-103 files

FreeBSD/src e878df0lib/libsys _libsys.h, sys/compat/freebsd32 freebsd32_systrace_args.c freebsd32_proto.h

Regen syscall tables after pdfork(2) and pdwait(2) additions
DeltaFile
+68-0sys/compat/freebsd32/freebsd32_systrace_args.c
+68-0sys/kern/systrace_args.c
+16-0sys/sys/sysproto.h
+9-0sys/compat/freebsd32/freebsd32_proto.h
+3-1sys/compat/freebsd32/freebsd32_syscall.h
+4-0lib/libsys/_libsys.h
+168-17 files not shown
+186-313 files

FreeBSD/src 6c82bf1lib/libc/gen exterr_cat_filenames.h

Regen for the fork and exit/wait exterror category addition
DeltaFile
+2-0lib/libc/gen/exterr_cat_filenames.h
+2-01 files

FreeBSD/src ec8e8fashare/man/man4 rights.4

rights.4: document CAP_PDWAIT

Noted by:       markj
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+3-0share/man/man4/rights.4
+3-01 files

FreeBSD/src f7b5688lib/libsys pdfork.2 Makefile.sys

Document pdrfork(2) and pdwait(2)

Reviewed by:    asomers, markj
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+81-8lib/libsys/pdfork.2
+4-2lib/libsys/Makefile.sys
+1-0lib/libsys/rfork.2
+1-0lib/libsys/wait.2
+87-104 files

FreeBSD/src 2d555eclib/libc/sys pdwait.c Symbol.map, lib/libsys Makefile.sys interposing_table.c

lib/libsys, lib/libc: export pdwait

Make pdwait(2) cancellable, same as all other wait*(2) syscalls wrappers.

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+20-0lib/libc/sys/pdwait.c
+15-0lib/libthr/thread/thr_syscalls.c
+4-0sys/sys/procdesc.h
+4-0lib/libc/sys/Symbol.map
+1-0lib/libsys/Makefile.sys
+1-0lib/libsys/interposing_table.c
+45-01 files not shown
+46-07 files

FreeBSD/src 4d70782sys/compat/freebsd32 freebsd32_misc.c, sys/kern kern_exit.c syscalls.master

Add pdwait(2)

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+105-0sys/kern/kern_exit.c
+31-0sys/compat/freebsd32/freebsd32_misc.c
+10-0sys/kern/syscalls.master
+4-0sys/kern/sys_procdesc.c
+2-0sys/sys/syscallsubr.h
+152-05 files

FreeBSD/src 0998487sys/kern kern_exit.c sys_procdesc.c

procdesc: postpone freeing the zombie' pid until procdesc is freed

Requested by:   asomers
Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+2-2sys/kern/kern_exit.c
+4-0sys/kern/sys_procdesc.c
+6-22 files

FreeBSD/src aa72df7sys/kern subr_capability.c, sys/sys caprights.h

sys: Add cap_pdwait_rights

Suggested by:   asomers
Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+1-0sys/kern/subr_capability.c
+1-0sys/sys/caprights.h
+2-02 files

FreeBSD/src a560abesys/security/audit audit_bsm.c

audit: handle AUE_PDWAIT

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+10-0sys/security/audit/audit_bsm.c
+10-01 files

FreeBSD/src 7fe33d5sys/kern kern_exit.c

kern/kern_exit.c: extract wait6_check_alive() helper

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+59-37sys/kern/kern_exit.c
+59-371 files

FreeBSD/src 2b67cfasys/kern kern_exit.c

kern/kern_exit.c: extract some helpers from proc_to_reap()

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+66-50sys/kern/kern_exit.c
+66-501 files

FreeBSD/src 109b9f4sys/kern kern_exit.c, sys/sys exterr_cat.h

kern/kern_exit.c: define the exterror category for exit/wait

Convert EINVALs in kern_exit.c into EXTERRORs.

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+25-14sys/kern/kern_exit.c
+1-0sys/sys/exterr_cat.h
+26-142 files

FreeBSD/src f10b4b6lib/libsys Symbol.sys.map, sys/sys procdesc.h

lib/libsys, lib/libc: export pdrfork(2)

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+4-0lib/libsys/Symbol.sys.map
+1-0sys/sys/procdesc.h
+5-02 files

FreeBSD/src 5c2ee61sys/kern kern_fork.c syscalls.master

sys: add pdrfork(2)

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+42-0sys/kern/kern_fork.c
+9-0sys/kern/syscalls.master
+51-02 files

FreeBSD/src d0d4b9bsys/bsm audit_kevents.h, sys/security/audit audit_bsm.c

sys: add AUE_PDRFORK

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+18-0sys/security/audit/audit_bsm.c
+1-0sys/bsm/audit_kevents.h
+19-02 files

FreeBSD/src 7211cd2sys/kern kern_fork.c, sys/sys exterr_cat.h

kern/kern_fork.c: define the exterror category for fork

Convert EINVALs in kern_fork.c into EXTERRORs.

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+18-17sys/kern/kern_fork.c
+1-0sys/sys/exterr_cat.h
+19-172 files

FreeBSD/src 472c32asys/kern kern_exit.c kern_fork.c

kern/kern_fork/exit.c: organize includes

Remove sys/cdefs.h.
Remove sys/param.h.
Order the sys/*.h includes alphabetically.

Reviewed by:    asomers, markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+15-17sys/kern/kern_exit.c
+8-10sys/kern/kern_fork.c
+23-272 files

FreeBSD/src f5acbacsys/kern kern_exit.c

kern/kern_exit.c: some style

Reviewed by:    asomers, markj
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+11-12sys/kern/kern_exit.c
+11-121 files

FreeBSD/src 6af3cf2sys/compat/freebsd32 freebsd32_misc.c

freebsd32_rusage_out(): bzero the compat32 structure

There is some padding on non-x86.  Unconditionally bzero the memory to
avoid a leak.

Noted by:       markj
Reviewed by:    markj
Tested by:      pho
Sponsored by:   The FreeBSD Foundation
MFC after:      1 week
Differential revision:  https://reviews.freebsd.org/D54592
DeltaFile
+1-0sys/compat/freebsd32/freebsd32_misc.c
+1-01 files

LLVM/project 9a0bca2llvm/lib/Transforms/InstCombine InstCombineSimplifyDemanded.cpp, llvm/test/Transforms/InstCombine simplify-demanded-fpclass.ll

InstCombine: Handle nsz in copysign SimplifyDemandedFPClass

If the only sign bit difference is for 0, fold through the source.
DeltaFile
+31-1llvm/lib/Transforms/InstCombine/InstCombineSimplifyDemanded.cpp
+2-4llvm/test/Transforms/InstCombine/simplify-demanded-fpclass.ll
+33-52 files

LLVM/project 78ce56cllvm/lib/Transforms/InstCombine InstCombineSimplifyDemanded.cpp

Address comments
DeltaFile
+3-3llvm/lib/Transforms/InstCombine/InstCombineSimplifyDemanded.cpp
+3-31 files

LLVM/project 025f150llvm/test/Transforms/InstCombine simplify-demanded-fpclass.ll

InstCombine: Add baseline tests for SimplifyDemandedFPClass copysign improvements

Prepare to support more folds and multiple uses.
DeltaFile
+651-0llvm/test/Transforms/InstCombine/simplify-demanded-fpclass.ll
+651-01 files

LLVM/project 0b24eacllvm/lib/Transforms/InstCombine InstCombineSimplifyDemanded.cpp, llvm/test/Transforms/InstCombine simplify-demanded-fpclass.ll

InstCombine: Improve single-use fneg(fabs(x)) SimplifyDemandedFPClass handling

Match the multi-use case's logic for understanding no-nan/no-inf context.
Also only apply the nsz handling in the single use case. alive2 seems to treat
nsz as nondeterministic for each use.
DeltaFile
+244-11llvm/test/Transforms/InstCombine/simplify-demanded-fpclass.ll
+74-20llvm/lib/Transforms/InstCombine/InstCombineSimplifyDemanded.cpp
+318-312 files

LLVM/project 2370bf2llvm/include/llvm/CodeGen SDPatternMatch.h, llvm/lib/CodeGen/SelectionDAG DAGCombiner.cpp

[DAG] Extend MinMax matchers to detect flippable sign (#177504)

Fixes #174328
DeltaFile
+115-0llvm/unittests/CodeGen/SelectionDAGPatternMatchTest.cpp
+68-0llvm/test/CodeGen/AArch64/abds.ll
+22-8llvm/include/llvm/CodeGen/SDPatternMatch.h
+8-8llvm/lib/CodeGen/SelectionDAG/DAGCombiner.cpp
+213-164 files

LLVM/project 61c1621mlir/lib/CAPI/Transforms Rewrite.cpp, mlir/lib/Dialect/ArmNeon/Transforms LowerContractToNeonPatterns.cpp

[MLIR] Fix GCC's `-Wreturn-type` warnings (#177654)

This patch fixes `-Wreturn-type` warnings which happens if MLIR is built
with GCC compiler (11.5 is used for detecting)


Founded errors
```
build/llvm-llvmorg-21.1.8/mlir/lib/CAPI/Transforms/Rewrite.cpp: In function ‘MlirGreedyRewriteStrictness mlirGreedyRewriteDriverConfigGetStrictness(MlirGreedyRewriteDriverConfig)’:
build/llvm-llvmorg-21.1.8/mlir/lib/CAPI/Transforms/Rewrite.cpp:399:1: warning: control reaches end of non-void function [-Wreturn-type]
  399 | }
      | ^
build/llvm-llvmorg-21.1.8/mlir/lib/CAPI/Transforms/Rewrite.cpp: In function ‘MlirGreedySimplifyRegionLevel mlirGreedyRewriteDriverConfigGetRegionSimplificationLevel(MlirGreedyRewriteDriverConfig)’:
build/llvm-llvmorg-21.1.8/mlir/lib/CAPI/Transforms/Rewrite.cpp:414:1: warning: control reaches end of non-void function [-Wreturn-type]
  414 | }
      | ^
build/llvm-llvmorg-21.1.8/mlir/lib/Dialect/GPU/IR/GPUDialect.cpp: In member function ‘mlir::Speculation::Speculatability mlir::gpu::SubgroupBroadcastOp::getSpeculatability()’:
build/llvm-llvmorg-21.1.8/mlir/lib/Dialect/GPU/IR/GPUDialect.cpp:2522:1: warning: control reaches end of non-void function [-Wreturn-type]
 2522 | }

    [20 lines not shown]
DeltaFile
+2-0mlir/lib/CAPI/Transforms/Rewrite.cpp
+2-0mlir/lib/Dialect/GPU/IR/GPUDialect.cpp
+1-0mlir/test/lib/Dialect/Test/TestOpDefs.cpp
+1-0mlir/lib/Dialect/Linalg/IR/LinalgOps.cpp
+1-0mlir/lib/Dialect/ArmNeon/Transforms/LowerContractToNeonPatterns.cpp
+7-05 files

OPNSense/core 3c86f5dsrc/etc/inc/plugins.inc.d radvd.inc

radvd: remove faulty condition introduced in 733f5057d0c

I'm not sure why it was there.  No address means no working radvd.
DeltaFile
+1-1src/etc/inc/plugins.inc.d/radvd.inc
+1-11 files

FreeBSD/ports 6920432lang/rust update.sh

lang/rust: Fix LLVM_VERSION

Fixes:  a802c571830fc166c61fea2e957944127458cde4
DeltaFile
+1-1lang/rust/update.sh
+1-11 files

LLVM/project 2297e0dllvm/lib/Transforms/Utils MoveAutoInit.cpp, llvm/test/Transforms/MoveAutoInit loop-store.ll

[MoveAutoInit] Fix for miscompilation for #150120 (#173961)

Fixes the miscompilation discussed for the PR #164882 as part of
generalizing the optimization for the issue #150120.

Without this commit, MoveAutoInit moves the store instruction to a
different branch which does not dominate the user dominator node. This
results in UB at runtime. The example in the test case is specifically
for an irreducible loop, in which all the predecessor may not dominate
user dominator head.

To fix this problem, we've introduced a new check to verify if the
predecessor of the user dominator node does in fact dominate user
dominator node before deciding that it is the node where the instruction
will be moved to.
DeltaFile
+59-0llvm/test/Transforms/MoveAutoInit/loop-store.ll
+2-1llvm/lib/Transforms/Utils/MoveAutoInit.cpp
+61-12 files