Linux-stable-mirror
August 2024
linux-stable-mirror@lists.linaro.org
- 504 participants
- 1324 discussions
[PATCH -stable,6.6.x 0/1] Netfilter fixes for -stable
by Pablo Neira Ayuso
Hi Greg, Sasha,
This batch contains a backport for recent fixes already upstream for 6.6.x.
The following list shows the backported patch, I am using original commit
IDs for reference:
1) cff3bd012a95 ("netfilter: nf_tables: prefer nft_chain_validate")
Only one patch for this -stable branch.
Please, apply,
Thanks.
Florian Westphal (1):
netfilter: nf_tables: prefer nft_chain_validate
net/netfilter/nf_tables_api.c | 154 +++-------------------------------
1 file changed, 13 insertions(+), 141 deletions(-)
--
2.30.2
8 months, 2 weeks
- 2
- 2
[PATCH 6.10.y] idpf: fix memleak in vport interrupt configuration
by Alexander Lobakin
From: Michal Kubiak <michal.kubiak(a)intel.com>
commit 3cc88e8405b8d55e0ff035e31971aadd6baee2b6 upstream.
The initialization of vport interrupt consists of two functions:
1) idpf_vport_intr_init() where a generic configuration is done
2) idpf_vport_intr_req_irq() where the irq for each q_vector is
requested.
The first function used to create a base name for each interrupt using
"kasprintf()" call. Unfortunately, although that call allocated memory
for a text buffer, that memory was never released.
Fix this by removing creating the interrupt base name in 1).
Instead, always create a full interrupt name in the function 2), because
there is no need to create a base name separately, considering that the
function 2) is never called out of idpf_vport_intr_init() context.
Fixes: d4d558718266 ("idpf: initialize interrupts and enable vport")
Cc: stable(a)vger.kernel.org # 6.7
Signed-off-by: Michal Kubiak <michal.kubiak(a)intel.com>
Reviewed-by: Pavan Kumar Linga <pavan.kumar.linga(a)intel.com>
Signed-off-by: Alexander Lobakin <aleksander.lobakin(a)intel.com>
Reviewed-by: Simon Horman <horms(a)kernel.org>
Tested-by: Krishneil Singh <krishneil.k.singh(a)intel.com>
Signed-off-by: Tony Nguyen <anthony.l.nguyen(a)intel.com>
Link: https://patch.msgid.link/20240806220923.3359860-3-anthony.l.nguyen@intel.com
Signed-off-by: Jakub Kicinski <kuba(a)kernel.org>
---
drivers/net/ethernet/intel/idpf/idpf_txrx.c | 19 ++++++++-----------
1 file changed, 8 insertions(+), 11 deletions(-)
diff --git a/drivers/net/ethernet/intel/idpf/idpf_txrx.c b/drivers/net/ethernet/intel/idpf/idpf_txrx.c
index b023704bbbda..ed68c7baefa3 100644
--- a/drivers/net/ethernet/intel/idpf/idpf_txrx.c
+++ b/drivers/net/ethernet/intel/idpf/idpf_txrx.c
@@ -3636,13 +3636,15 @@ void idpf_vport_intr_update_itr_ena_irq(struct idpf_q_vector *q_vector)
/**
* idpf_vport_intr_req_irq - get MSI-X vectors from the OS for the vport
* @vport: main vport structure
- * @basename: name for the vector
*/
-static int idpf_vport_intr_req_irq(struct idpf_vport *vport, char *basename)
+static int idpf_vport_intr_req_irq(struct idpf_vport *vport)
{
struct idpf_adapter *adapter = vport->adapter;
+ const char *drv_name, *if_name, *vec_name;
int vector, err, irq_num, vidx;
- const char *vec_name;
+
+ drv_name = dev_driver_string(&adapter->pdev->dev);
+ if_name = netdev_name(vport->netdev);
for (vector = 0; vector < vport->num_q_vectors; vector++) {
struct idpf_q_vector *q_vector = &vport->q_vectors[vector];
@@ -3659,8 +3661,8 @@ static int idpf_vport_intr_req_irq(struct idpf_vport *vport, char *basename)
else
continue;
- q_vector->name = kasprintf(GFP_KERNEL, "%s-%s-%d",
- basename, vec_name, vidx);
+ q_vector->name = kasprintf(GFP_KERNEL, "%s-%s-%s-%d", drv_name,
+ if_name, vec_name, vidx);
err = request_irq(irq_num, idpf_vport_intr_clean_queues, 0,
q_vector->name, q_vector);
@@ -4170,7 +4172,6 @@ int idpf_vport_intr_alloc(struct idpf_vport *vport)
*/
int idpf_vport_intr_init(struct idpf_vport *vport)
{
- char *int_name;
int err;
err = idpf_vport_intr_init_vec_idx(vport);
@@ -4184,11 +4185,7 @@ int idpf_vport_intr_init(struct idpf_vport *vport)
if (err)
goto unroll_vectors_alloc;
- int_name = kasprintf(GFP_KERNEL, "%s-%s",
- dev_driver_string(&vport->adapter->pdev->dev),
- vport->netdev->name);
-
- err = idpf_vport_intr_req_irq(vport, int_name);
+ err = idpf_vport_intr_req_irq(vport);
if (err)
goto unroll_vectors_alloc;
--
2.46.0
8 months, 2 weeks
- 2
- 1
[PATCH for 5.15 stable] btrfs: fix corruption after buffer fault in during direct IO append write
by fdmanana＠kernel.org
From: Filipe Manana <fdmanana(a)suse.com>
commit 939b656bc8ab203fdbde26ccac22bcb7f0985be5 upstream.
During an append (O_APPEND write flag) direct IO write if the input buffer
was not previously faulted in, we can corrupt the file in a way that the
final size is unexpected and it includes an unexpected hole.
The problem happens like this:
1) We have an empty file, with size 0, for example;
2) We do an O_APPEND direct IO with a length of 4096 bytes and the input
buffer is not currently faulted in;
3) We enter btrfs_direct_write(), lock the inode and call
generic_write_checks(), which calls generic_write_checks_count(), and
that function sets the iocb position to 0 with the following code:
if (iocb->ki_flags & IOCB_APPEND)
iocb->ki_pos = i_size_read(inode);
4) We call btrfs_dio_write() and enter into iomap, which will end up
calling btrfs_dio_iomap_begin() and that calls
btrfs_get_blocks_direct_write(), where we update the i_size of the
inode to 4096 bytes;
5) After btrfs_dio_iomap_begin() returns, iomap will attempt to access
the page of the write input buffer (at iomap_dio_bio_iter(), with a
call to bio_iov_iter_get_pages()) and fail with -EFAULT, which gets
returned to btrfs at btrfs_direct_write() via btrfs_dio_write();
6) At btrfs_direct_write() we get the -EFAULT error, unlock the inode,
fault in the write buffer and then goto to the label 'relock';
7) We lock again the inode, do all the necessary checks again and call
again generic_write_checks(), which calls generic_write_checks_count()
again, and there we set the iocb's position to 4K, which is the current
i_size of the inode, with the following code pointed above:
if (iocb->ki_flags & IOCB_APPEND)
iocb->ki_pos = i_size_read(inode);
8) Then we go again to btrfs_dio_write() and enter iomap and the write
succeeds, but it wrote to the file range [4K, 8K[, leaving a hole in
the [0, 4K[ range and an i_size of 8K, which goes against the
expections of having the data written to the range [0, 4K[ and get an
i_size of 4K.
Fix this by not unlocking the inode before faulting in the input buffer,
in case we get -EFAULT or an incomplete write, and not jumping to the
'relock' label after faulting in the buffer - instead jump to a location
immediately before calling iomap, skipping all the write checks and
relocking. This solves this problem and it's fine even in case the input
buffer is memory mapped to the same file range, since only holding the
range locked in the inode's io tree can cause a deadlock, it's safe to
keep the inode lock (VFS lock), as was fixed and described in commit
51bd9563b678 ("btrfs: fix deadlock due to page faults during direct IO
reads and writes").
A sample reproducer provided by a reporter is the following:
$ cat test.c
#ifndef _GNU_SOURCE
#define _GNU_SOURCE
#endif
#include <fcntl.h>
#include <stdio.h>
#include <sys/mman.h>
#include <sys/stat.h>
#include <unistd.h>
int main(int argc, char *argv[])
{
if (argc < 2) {
fprintf(stderr, "Usage: %s <test file>\n", argv[0]);
return 1;
}
int fd = open(argv[1], O_WRONLY | O_CREAT | O_TRUNC | O_DIRECT |
O_APPEND, 0644);
if (fd < 0) {
perror("creating test file");
return 1;
}
char *buf = mmap(NULL, 4096, PROT_READ,
MAP_PRIVATE | MAP_ANONYMOUS, -1, 0);
ssize_t ret = write(fd, buf, 4096);
if (ret < 0) {
perror("pwritev2");
return 1;
}
struct stat stbuf;
ret = fstat(fd, &stbuf);
if (ret < 0) {
perror("stat");
return 1;
}
printf("size: %llu\n", (unsigned long long)stbuf.st_size);
return stbuf.st_size == 4096 ? 0 : 1;
}
A test case for fstests will be sent soon.
Reported-by: Hanna Czenczek <hreitz(a)redhat.com>
Link: https://lore.kernel.org/linux-btrfs/0b841d46-12fe-4e64-9abb-871d8d0de271@re…
Fixes: 8184620ae212 ("btrfs: fix lost file sync on direct IO write with nowait and dsync iocb")
Signed-off-by: Filipe Manana <fdmanana(a)suse.com>
---
fs/btrfs/ctree.h | 1 +
fs/btrfs/file.c | 55 ++++++++++++++++++++++++++++++++++++------------
2 files changed, 43 insertions(+), 13 deletions(-)
diff --git a/fs/btrfs/ctree.h b/fs/btrfs/ctree.h
index 17ebcf19b444..f19c6aa3ea4b 100644
--- a/fs/btrfs/ctree.h
+++ b/fs/btrfs/ctree.h
@@ -1383,6 +1383,7 @@ struct btrfs_drop_extents_args {
struct btrfs_file_private {
void *filldir_buf;
u64 last_index;
+ bool fsync_skip_inode_lock;
};
diff --git a/fs/btrfs/file.c b/fs/btrfs/file.c
index eae622ef4c6d..7ca49c02e8f8 100644
--- a/fs/btrfs/file.c
+++ b/fs/btrfs/file.c
@@ -1983,22 +1983,38 @@ static ssize_t btrfs_direct_write(struct kiocb *iocb, struct iov_iter *from)
* So here we disable page faults in the iov_iter and then retry if we
* got -EFAULT, faulting in the pages before the retry.
*/
+again:
from->nofault = true;
dio = __iomap_dio_rw(iocb, from, &btrfs_dio_iomap_ops, &btrfs_dio_ops,
IOMAP_DIO_PARTIAL, written);
from->nofault = false;
- /*
- * iomap_dio_complete() will call btrfs_sync_file() if we have a dsync
- * iocb, and that needs to lock the inode. So unlock it before calling
- * iomap_dio_complete() to avoid a deadlock.
- */
- btrfs_inode_unlock(inode, ilock_flags);
-
- if (IS_ERR_OR_NULL(dio))
+ if (IS_ERR_OR_NULL(dio)) {
err = PTR_ERR_OR_ZERO(dio);
- else
+ } else {
+ struct btrfs_file_private stack_private = { 0 };
+ struct btrfs_file_private *private;
+ const bool have_private = (file->private_data != NULL);
+
+ if (!have_private)
+ file->private_data = &stack_private;
+
+ /*
+ * If we have a synchoronous write, we must make sure the fsync
+ * triggered by the iomap_dio_complete() call below doesn't
+ * deadlock on the inode lock - we are already holding it and we
+ * can't call it after unlocking because we may need to complete
+ * partial writes due to the input buffer (or parts of it) not
+ * being already faulted in.
+ */
+ private = file->private_data;
+ private->fsync_skip_inode_lock = true;
err = iomap_dio_complete(dio);
+ private->fsync_skip_inode_lock = false;
+
+ if (!have_private)
+ file->private_data = NULL;
+ }
/* No increment (+=) because iomap returns a cumulative value. */
if (err > 0)
@@ -2025,10 +2041,12 @@ static ssize_t btrfs_direct_write(struct kiocb *iocb, struct iov_iter *from)
} else {
fault_in_iov_iter_readable(from, left);
prev_left = left;
- goto relock;
+ goto again;
}
}
+ btrfs_inode_unlock(inode, ilock_flags);
+
/* If 'err' is -ENOTBLK then it means we must fallback to buffered IO. */
if ((err < 0 && err != -ENOTBLK) || !iov_iter_count(from))
goto out;
@@ -2177,6 +2195,7 @@ static inline bool skip_inode_logging(const struct btrfs_log_ctx *ctx)
*/
int btrfs_sync_file(struct file *file, loff_t start, loff_t end, int datasync)
{
+ struct btrfs_file_private *private = file->private_data;
struct dentry *dentry = file_dentry(file);
struct inode *inode = d_inode(dentry);
struct btrfs_fs_info *fs_info = btrfs_sb(inode->i_sb);
@@ -2186,6 +2205,7 @@ int btrfs_sync_file(struct file *file, loff_t start, loff_t end, int datasync)
int ret = 0, err;
u64 len;
bool full_sync;
+ const bool skip_ilock = (private ? private->fsync_skip_inode_lock : false);
trace_btrfs_sync_file(file, datasync);
@@ -2213,7 +2233,10 @@ int btrfs_sync_file(struct file *file, loff_t start, loff_t end, int datasync)
if (ret)
goto out;
- btrfs_inode_lock(inode, BTRFS_ILOCK_MMAP);
+ if (skip_ilock)
+ down_write(&BTRFS_I(inode)->i_mmap_lock);
+ else
+ btrfs_inode_lock(inode, BTRFS_ILOCK_MMAP);
atomic_inc(&root->log_batch);
@@ -2245,7 +2268,10 @@ int btrfs_sync_file(struct file *file, loff_t start, loff_t end, int datasync)
*/
ret = start_ordered_ops(inode, start, end);
if (ret) {
- btrfs_inode_unlock(inode, BTRFS_ILOCK_MMAP);
+ if (skip_ilock)
+ up_write(&BTRFS_I(inode)->i_mmap_lock);
+ else
+ btrfs_inode_unlock(inode, BTRFS_ILOCK_MMAP);
goto out;
}
@@ -2337,7 +2363,10 @@ int btrfs_sync_file(struct file *file, loff_t start, loff_t end, int datasync)
* file again, but that will end up using the synchronization
* inside btrfs_sync_log to keep things safe.
*/
- btrfs_inode_unlock(inode, BTRFS_ILOCK_MMAP);
+ if (skip_ilock)
+ up_write(&BTRFS_I(inode)->i_mmap_lock);
+ else
+ btrfs_inode_unlock(inode, BTRFS_ILOCK_MMAP);
if (ret == BTRFS_NO_LOG_SYNC) {
ret = btrfs_end_transaction(trans);
--
2.43.0
8 months, 2 weeks
- 2
- 1
[PATCH 6.10 000/809] 6.10.3-rc1 review
by Greg Kroah-Hartman
This is the start of the stable review cycle for the 6.10.3 release.
There are 809 patches in this series, all will be posted as a response
to this one. If anyone has any issues with these being applied, please
let me know.
Responses should be made by Thu, 01 Aug 2024 15:14:54 +0000.
Anything received after that time might be too late.
The whole patch series can be found in one patch at:
https://www.kernel.org/pub/linux/kernel/v6.x/stable-review/patch-6.10.3-rc1…
or in the git tree and branch at:
git://git.kernel.org/pub/scm/linux/kernel/git/stable/linux-stable-rc.git linux-6.10.y
and the diffstat can be found below.
thanks,
greg k-h
-------------
Pseudo-Shortlog of commits:
Greg Kroah-Hartman <gregkh(a)linuxfoundation.org>
Linux 6.10.3-rc1
James Clark <james.clark(a)linaro.org>
perf dso: Fix build when libunwind is enabled
Karthikeyan Periyasamy <quic_periyasa(a)quicinc.com>
wifi: ath12k: fix mbssid max interface advertisement
Seth Forshee (DigitalOcean) <sforshee(a)kernel.org>
fs: don't allow non-init s_user_ns for filesystems without FS_USERNS_MOUNT
Jarkko Nikula <jarkko.nikula(a)linux.intel.com>
i3c: mipi-i3c-hci: Fix number of DAT/DCT entries for HCI versions < 1.1
Leon Romanovsky <leon(a)kernel.org>
nvme-pci: add missing condition check for existence of mapped data
Georgia Garcia <georgia.garcia(a)canonical.com>
apparmor: unpack transition table if dfa is not present
Ming Lei <ming.lei(a)redhat.com>
ublk: fix UBLK_CMD_DEL_DEV_ASYNC handling
Pavel Begunkov <asml.silence(a)gmail.com>
io_uring: fix io_match_task must_hold
Rafael J. Wysocki <rafael.j.wysocki(a)intel.com>
thermal: core: Back off when polling thermal zones on errors
Rafael J. Wysocki <rafael.j.wysocki(a)intel.com>
thermal: trip: Split thermal_zone_device_set_mode()
Artem Chernyshev <artem.chernyshev(a)red-soft.ru>
iommu: sprd: Avoid NULL deref in sprd_iommu_hw_en
Thomas Richter <tmricht(a)linux.ibm.com>
s390/cpum_cf: Fix endless loop in CF_DIAG event stop
Vasily Gorbik <gor(a)linux.ibm.com>
s390/setup: Fix __pa/__va for modules under non-GPL licenses
Gerd Bayer <gbayer(a)linux.ibm.com>
s390/pci: Allow allocation of more than 1 MSI interrupt
Gerd Bayer <gbayer(a)linux.ibm.com>
s390/pci: Refactor arch_setup_msi_irqs()
ethanwu <ethanwu(a)synology.com>
ceph: fix incorrect kmalloc size of pagevec mempool
Anna-Maria Behnsen <anna-maria(a)linutronix.de>
timers/migration: Do not rely always on group->parent
Dan Carpenter <dan.carpenter(a)linaro.org>
ASoC: TAS2781: Fix tasdev_load_calibrated_data()
Pierre-Louis Bossart <pierre-louis.bossart(a)linux.intel.com>
ASoC: Intel: use soc_intel_is_byt_cr() only when IOSF_MBI is reachable
Michal Wajdeczko <michal.wajdeczko(a)intel.com>
drm/xe/pf: Limit fair VF LMEM provisioning
Ashutosh Dixit <ashutosh.dixit(a)intel.com>
drm/xe/exec: Fix minor bug related to xe_sync_entry_cleanup
Conor Dooley <conor.dooley(a)microchip.com>
spi: spidev: add correct compatible for Rohm BH2228FV
Venkata Prasad Potturu <venkataprasad.potturu(a)amd.com>
ASoC: sof: amd: fix for firmware reload failure in Vangogh platform
Curtis Malainey <cujomalainey(a)chromium.org>
ASoC: Intel: Fix RT5650 SSP lookup
Pierre-Louis Bossart <pierre-louis.bossart(a)linux.intel.com>
ASOC: SOF: Intel: hda-loader: only wait for HDaudio IOC for IPC4 devices
Bart Van Assche <bvanassche(a)acm.org>
nvme-pci: Fix the instructions for disabling power management
Steve Wilkins <steve.wilkins(a)raymarine.com>
spi: microchip-core: ensure TX and RX FIFOs are empty at start of a transfer
Steve Wilkins <steve.wilkins(a)raymarine.com>
spi: microchip-core: fix init function not setting the master and motorola modes
Steve Wilkins <steve.wilkins(a)raymarine.com>
spi: microchip-core: only disable SPI controller when register value change requires it
Steve Wilkins <steve.wilkins(a)raymarine.com>
spi: microchip-core: defer asserting chip select until just before write to TX FIFO
Naga Sureshkumar Relli <nagasuresh.relli(a)microchip.com>
spi: microchip-core: fix the issues in the isr
Daniel Baluta <daniel.baluta(a)nxp.com>
ASoC: SOF: imx8m: Fix DSP control regmap retrieval
Markus Elfring <elfring(a)users.sourceforge.net>
auxdisplay: ht16k33: Drop reference after LED registration
Al Viro <viro(a)zeniv.linux.org.uk>
lirc: rc_dev_get_from_fd(): fix file leak
Al Viro <viro(a)zeniv.linux.org.uk>
powerpc: fix a file leak in kvm_vcpu_ioctl_enable_cap()
Xiao Liang <shaw.leon(a)gmail.com>
apparmor: Fix null pointer deref when receiving skb during sock creation
Dan Carpenter <dan.carpenter(a)linaro.org>
mISDN: Fix a use after free in hfcmulti_tx()
Stanislav Fomichev <sdf(a)fomichev.me>
xsk: Require XDP_UMEM_TX_METADATA_LEN to actuate tx_metadata_len
Fred Li <dracodingfly(a)gmail.com>
bpf: Fix a segment issue when downgrading gso_size
Breno Leitao <leitao(a)debian.org>
net: mediatek: Fix potential NULL pointer dereference in dummy net_device handling
Petr Machata <petrm(a)nvidia.com>
net: nexthop: Initialize all fields in dumped nexthops
Simon Horman <horms(a)kernel.org>
net: stmmac: Correct byte order of perfect_match
Hangbin Liu <liuhangbin(a)gmail.com>
selftests: forwarding: skip if kernel not support setting bridge fdb learning limit
Shigeru Yoshida <syoshida(a)redhat.com>
tipc: Return non-zero value from tipc_udp_addr2str() on error
David Howells <dhowells(a)redhat.com>
netfs: Fix writeback that needs to go to both server and cache
Florian Westphal <fw(a)strlen.de>
netfilter: nft_set_pipapo_avx2: disable softinterrupts
Wojciech Drewek <wojciech.drewek(a)intel.com>
ice: Fix recipe read procedure
Johannes Berg <johannes.berg(a)intel.com>
net: bonding: correctly annotate RCU in bond_should_notify_peers()
Ido Schimmel <idosch(a)nvidia.com>
ipv4: Fix incorrect source address in Record Route option
Gregory CLEMENT <gregory.clement(a)bootlin.com>
MIPS: SMP-CPS: Fix address for GCR_ACCESS register for CM3 and later
Liwei Song <liwei.song.lsong(a)gmail.com>
tools/resolve_btfids: Fix comparison of distinct pointer types warning in resolve_btfids
Hou Tao <houtao1(a)huawei.com>
bpf, events: Use prog to emit ksymbol event for main program
Lance Richardson <rlance(a)google.com>
dma: fix call order in dmam_free_coherent
Michal Luczaj <mhal(a)rbox.co>
af_unix: Disable MSG_OOB handling for sockets in sockmap/sockhash
Andrii Nakryiko <andrii(a)kernel.org>
libbpf: Fix no-args func prototype BTF dumping syntax
Puranjay Mohan <puranjay(a)kernel.org>
selftests/bpf: fexit_sleep: Fix stack allocation for arm64
Masahiro Yamada <masahiroy(a)kernel.org>
kbuild: avoid build error when single DTB is turned into composite DTB
Chao Yu <chao(a)kernel.org>
f2fs: fix to update user block counts in block_operations()
Daejun Park <daejun7.park(a)samsung.com>
f2fs: fix null reference error when checking end of zone
Claudiu Beznea <claudiu.beznea.uj(a)bp.renesas.com>
watchdog: rzg2l_wdt: Check return status of pm_runtime_put()
Claudiu Beznea <claudiu.beznea.uj(a)bp.renesas.com>
watchdog: rzg2l_wdt: Use pm_runtime_resume_and_get()
Sheng Yong <shengyong(a)oppo.com>
f2fs: fix start segno of large section
Johannes Berg <johannes.berg(a)intel.com>
um: time-travel: fix signal blocking race/hang
David Gow <davidgow(a)google.com>
arch: um: rust: Use the generated target.json again
Johannes Berg <johannes.berg(a)intel.com>
um: time-travel: fix time-travel-start option
Sean Anderson <sean.anderson(a)linux.dev>
phy: zynqmp: Enable reference clock correctly
Ma Ke <make24(a)iscas.ac.cn>
phy: cadence-torrent: Check return value on register read
Cristian Ciocaltea <cristian.ciocaltea(a)collabora.com>
phy: phy-rockchip-samsung-hdptx: Select CONFIG_MFD_SYSCON
Vignesh Raghavendra <vigneshr(a)ti.com>
dmaengine: ti: k3-udma: Fix BCHAN count with UHC and HC channels
Jeongjun Park <aha310510(a)gmail.com>
jfs: Fix array-index-out-of-bounds in diFree
Douglas Anderson <dianders(a)chromium.org>
kdb: Use the passed prompt in kdb_position_cursor()
Arnd Bergmann <arnd(a)arndb.de>
kdb: address -Wformat-security warnings
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
phy: qcom: qmp-pcie: restore compatibility with existing DTs
Chao Yu <chao(a)kernel.org>
f2fs: fix to truncate preallocated blocks in f2fs_file_open()
Linus Torvalds <torvalds(a)linux-foundation.org>
minmax: scsi: fix mis-use of 'clamp()' in sr.c
WangYuli <wangyuli(a)uniontech.com>
Bluetooth: btusb: Add Realtek RTL8852BE support ID 0x13d3:0x3591
Hilda Wu <hildawu(a)realtek.com>
Bluetooth: btusb: Add RTL8852BE device 0489:e125 to device tables
Ilya Dryomov <idryomov(a)gmail.com>
rbd: don't assume RBD_LOCK_STATE_LOCKED for exclusive mappings
Ilya Dryomov <idryomov(a)gmail.com>
rbd: rename RBD_LOCK_STATE_RELEASING and releasing_wait
Dragan Simic <dsimic(a)manjaro.org>
drm/panfrost: Mark simple_ondemand governor as softdep
Lucas Stach <l.stach(a)pengutronix.de>
drm/etnaviv: don't block scheduler when GPU is still active
Jiaxun Yang <jiaxun.yang(a)flygoat.com>
MIPS: Loongson64: Test register availability before use
Jiaxun Yang <jiaxun.yang(a)flygoat.com>
MIPS: Loongson64: reset: Prioritise firmware service
Jiaxun Yang <jiaxun.yang(a)flygoat.com>
MIPS: Loongson64: Remove memory node for builtin-dtb
Jiaxun Yang <jiaxun.yang(a)flygoat.com>
MIPS: Loongson64: env: Hook up Loongsson-2K
Jiaxun Yang <jiaxun.yang(a)flygoat.com>
MIPS: dts: loongson: Fix GMAC phy node
Jiaxun Yang <jiaxun.yang(a)flygoat.com>
MIPS: ip30: ip30-console: Add missing include
Jiaxun Yang <jiaxun.yang(a)flygoat.com>
MIPS: dts: loongson: Add ISA node
Aleksandr Mishin <amishin(a)t-argos.ru>
remoteproc: imx_rproc: Fix refcount mistake in imx_rproc_addr_init
Aleksandr Mishin <amishin(a)t-argos.ru>
remoteproc: imx_rproc: Skip over memory region when node value is NULL
Gwenael Treuveur <gwenael.treuveur(a)foss.st.com>
remoteproc: stm32_rproc: Fix mailbox interrupts queuing
Ilya Dryomov <idryomov(a)gmail.com>
rbd: don't assume rbd_is_lock_owner() for exclusive mappings
Eric Biggers <ebiggers(a)kernel.org>
dm-verity: fix dm_is_verity_target() when dm-verity is builtin
Michael Ellerman <mpe(a)ellerman.id.au>
selftests/sigaltstack: Fix ppc64 GCC build
Kim Phillips <kim.phillips(a)amd.com>
crypto: ccp - Fix null pointer dereference in __sev_snp_shutdown_locked
Bart Van Assche <bvanassche(a)acm.org>
RDMA/iwcm: Fix a use-after-free related to destroying CM IDs
Jiaxun Yang <jiaxun.yang(a)flygoat.com>
platform: mips: cpu_hwmon: Disable driver on unsupported hardware
Peter Ujfalusi <peter.ujfalusi(a)linux.intel.com>
ASoC: SOF: ipc4-topology: Use correct queue_id for requesting input pin format
Krzysztof Kozlowski <krzysztof.kozlowski(a)linaro.org>
ASoC: codecs: wcd939x: Fix typec mux and switch leak during device removal
Manivannan Sadhasivam <manivannan.sadhasivam(a)linaro.org>
bus: mhi: ep: Do not allocate memory for MHI objects from DMA zone
Thomas Gleixner <tglx(a)linutronix.de>
watchdog/perf: properly initialize the turbo mode timestamp and rearm counter
Joy Chakraborty <joychakr(a)google.com>
rtc: abx80x: Fix return value of nvmem callback on read
Joy Chakraborty <joychakr(a)google.com>
rtc: isl1208: Fix return value of nvmem callbacks
Imre Deak <imre.deak(a)intel.com>
drm/i915/dp: Don't switch the LTTPR mode on an active link
Imre Deak <imre.deak(a)intel.com>
drm/i915/dp: Reset intel_dp->link_trained before retraining the link
Ma Ke <make24(a)iscas.ac.cn>
drm/amd/amdgpu: Fix uninitialized variable warnings
Tim Huang <tim.huang(a)amd.com>
drm/amdgpu: add missed harvest check for VCN IP v4/v5
ZhenGuo Yin <zhenguo.yin(a)amd.com>
drm/amdgpu: reset vm state machine after gpu reset(vram lost)
Wayne Lin <Wayne.Lin(a)amd.com>
drm/dp_mst: Fix all mstb marked as not probed after suspend/resume
Thomas Zimmermann <tzimmermann(a)suse.de>
drm/udl: Remove DRM_CONNECTOR_POLL_HPD
Alex Deucher <alexander.deucher(a)amd.com>
drm/amdgpu/sdma5.2: Update wptr registers as well as doorbell
Nitin Gote <nitin.r.gote(a)intel.com>
drm/i915/gt: Do not consider preemption during execlists_dequeue for gen8
Adrian Hunter <adrian.hunter(a)intel.com>
perf/x86/intel/pt: Fix a topa_entry base address calculation
Marco Cavenati <cavenati.marco(a)gmail.com>
perf/x86/intel/pt: Fix topa_entry base length
Kan Liang <kan.liang(a)linux.intel.com>
perf/x86/intel/ds: Fix non 0 retire latency on Raptorlake
Kan Liang <kan.liang(a)linux.intel.com>
perf/x86/intel/uncore: Fix the bits of the CHA extended umask for SPR
Kan Liang <kan.liang(a)linux.intel.com>
perf stat: Fix the hard-coded metrics calculation on the hybrid
Frederic Weisbecker <frederic(a)kernel.org>
perf: Fix event leak upon exec and file release
Frederic Weisbecker <frederic(a)kernel.org>
perf: Fix event leak upon exit
Nilesh Javali <njavali(a)marvell.com>
scsi: qla2xxx: validate nvme_local_port correctly
Shreyas Deodhar <sdeodhar(a)marvell.com>
scsi: qla2xxx: Complete command early within lock
Quinn Tran <qutran(a)marvell.com>
scsi: qla2xxx: Fix flash read failure
Quinn Tran <qutran(a)marvell.com>
scsi: qla2xxx: Reduce fabric scan duplicate code
Quinn Tran <qutran(a)marvell.com>
scsi: qla2xxx: Use QP lock to search for bsg
Shreyas Deodhar <sdeodhar(a)marvell.com>
scsi: qla2xxx: Fix for possible memory corruption
Quinn Tran <qutran(a)marvell.com>
scsi: qla2xxx: Unable to act on RSCN for port online
Manish Rangankar <mrangankar(a)marvell.com>
scsi: qla2xxx: During vport delete send async logout explicitly
Justin Tee <justin.tee(a)broadcom.com>
scsi: lpfc: Allow DEVICE_RECOVERY mode after RSCN receipt if in PRLI_ISSUE state
Joy Chakraborty <joychakr(a)google.com>
rtc: cmos: Fix return value of nvmem callbacks
Tvrtko Ursulin <tvrtko.ursulin(a)igalia.com>
mm/numa_balancing: teach mpol_to_str about the balancing mode
Shenwei Wang <shenwei.wang(a)nxp.com>
irqchip/imx-irqsteer: Handle runtime power management correctly
Mateusz Jończyk <mat.jonczyk(a)o2.pl>
md/raid1: set max_sectors during early return from choose_slow_rdev()
Herve Codina <herve.codina(a)bootlin.com>
irqdomain: Fixed unbalanced fwnode get and put
Zijun Hu <quic_zijuhu(a)quicinc.com>
devres: Fix memory leakage caused by driver API devm_free_percpu()
Zijun Hu <quic_zijuhu(a)quicinc.com>
devres: Fix devm_krealloc() wasting memory
Yijie Yang <quic_yijiyang(a)quicinc.com>
dt-bindings: phy: qcom,qmp-usb: fix spelling error
Ahmed Zaki <ahmed.zaki(a)intel.com>
ice: Add a per-VF limit on number of FDIR filters
Bailey Forrest <bcf(a)google.com>
gve: Fix an edge case for TSO skb validity check
Zijun Hu <quic_zijuhu(a)quicinc.com>
kobject_uevent: Fix OOB access within zap_modalias_env()
Will Deacon <will(a)kernel.org>
arm64: mm: Fix lockless walks with static and dynamic page-table folding
Takashi Iwai <tiwai(a)suse.de>
ASoC: amd: yc: Support mic on Lenovo Thinkpad E16 Gen 2
Peter Ujfalusi <peter.ujfalusi(a)linux.intel.com>
ASoC: SOF: ipc4-topology: Preserve the DMA Link ID for ChainDMA on unprepare
Peter Ujfalusi <peter.ujfalusi(a)linux.intel.com>
ASoC: SOF: ipc4-topology: Only handle dai_config with HW_PARAMS for ChainDMA
Suren Baghdasaryan <surenb(a)google.com>
alloc_tag: outline and export free_reserved_page()
Nathan Chancellor <nathan(a)kernel.org>
kbuild: Fix '-S -c' in x86 stack protector scripts
Ross Lagerwall <ross.lagerwall(a)citrix.com>
decompress_bunzip2: fix rare decompression failure
Ram Tummala <rtummala(a)nvidia.com>
mm: fix old/young bit handling in the faulting path
Yang Yang <yang.yang(a)vivo.com>
block: fix deadlock between sd_remove & sd_release
Krzysztof Kozlowski <krzysztof.kozlowski(a)linaro.org>
clk: samsung: fix getting Exynos4 fin_pll rate from external clocks
Fedor Pchelkin <pchelkin(a)ispras.ru>
ubi: eba: properly rollback inside self_check_eba
Bastien Curutchet <bastien.curutchet(a)bootlin.com>
clk: davinci: da8xx-cfgchip: Initialize clk_init_data before use
Ryusuke Konishi <konishi.ryusuke(a)gmail.com>
nilfs2: handle inconsistent state in nilfs_btnode_create_block()
Joy Zou <joy.zou(a)nxp.com>
dmaengine: fsl-edma: change the memory access from local into remote mode in i.MX 8QM
Sunmin Jeong <s_min.jeong(a)samsung.com>
f2fs: use meta inode for GC of COW file
Sunmin Jeong <s_min.jeong(a)samsung.com>
f2fs: use meta inode for GC of atomic file
Chao Yu <chao(a)kernel.org>
f2fs: fix return value of f2fs_convert_inline_inode()
Chao Yu <chao(a)kernel.org>
f2fs: fix to don't dirty inode for readonly filesystem
Chao Yu <chao(a)kernel.org>
f2fs: fix to force buffered IO on inline_data inode
Herve Codina <herve.codina(a)bootlin.com>
ASoC: fsl: fsl_qmc_audio: Check devm_kasprintf() returned value
Saurav Kashyap <skashyap(a)marvell.com>
scsi: qla2xxx: Return ENOBUFS if sg_cnt is more than one for ELS cmds
Huacai Chen <chenhuacai(a)kernel.org>
fs/ntfs3: Update log->page_{mask,bits} if log->page_size changed
Li Zhijian <lizhijian(a)fujitsu.com>
mm/page_alloc: fix pcp->count race between drain_pages_zone() vs __rmqueue_pcplist()
Gao Xiang <xiang(a)kernel.org>
erofs: fix race in z_erofs_get_gbuf()
Qiang Ma <maqianga(a)uniontech.com>
efi/libstub: Zero initialize heap allocated struct screen_info
Johannes Berg <johannes.berg(a)intel.com>
hostfs: fix dev_t handling
tuhaowen <tuhaowen(a)uniontech.com>
dev/parport: fix the array out-of-bounds risk
Reka Norman <rekanorman(a)chromium.org>
xhci: Apply XHCI_RESET_TO_DEFAULT quirk to TGL
Carlos Llamas <cmllamas(a)google.com>
binder: fix hang of unregistered readers
Huacai Chen <chenhuacai(a)kernel.org>
PCI: loongson: Enable MSI in LS7A Root Complex
Manivannan Sadhasivam <manivannan.sadhasivam(a)linaro.org>
PCI: rockchip: Use GPIOD_OUT_LOW flag while requesting ep_gpio
Niklas Cassel <cassel(a)kernel.org>
PCI: dw-rockchip: Fix initial PERST# GPIO value
Wei Liu <wei.liu(a)kernel.org>
PCI: hv: Return zero, not garbage, when reading PCI_INTERRUPT_PIN
Lukas Wunner <lukas(a)wunner.de>
PCI/DPC: Fix use-after-free on concurrent DPC and hot-removal
John David Anglin <dave(a)mx3210.local>
parisc: Fix warning at drivers/pci/msi/msi.h:121
Ilpo Järvinen <ilpo.jarvinen(a)linux.intel.com>
hwrng: amd - Convert PCIBIOS_* return codes to errnos
Thomas Huth <thuth(a)redhat.com>
drm/fbdev-dma: Fix framebuffer mode for big endian devices
Thomas Zimmermann <tzimmermann(a)suse.de>
fbdev: vesafb: Detect VGA compatibility from screen info's VESA attributes
Alan Stern <stern(a)rowland.harvard.edu>
tools/memory-model: Fix bug in lock.cat
wangdicheng <wangdicheng(a)kylinos.cn>
ALSA: usb-audio: Add a quirk for Sonix HD USB Camera
Takashi Iwai <tiwai(a)suse.de>
ALSA: usb-audio: Move HD Webcam quirk to the right place
wangdicheng <wangdicheng(a)kylinos.cn>
ALSA: usb-audio: Fix microphone sound on HD webcam.
Takashi Iwai <tiwai(a)suse.de>
ALSA: ump: Force 1 Group for MIDI1 FBs
Takashi Iwai <tiwai(a)suse.de>
ALSA: ump: Don't update FB name for static blocks
Takashi Sakamoto <o-takashi(a)sakamocchi.jp>
ALSA: firewire-lib: fix wrong value as length of header for CIP_NO_HEADER case
Luke D. Jones <luke(a)ljones.dev>
ALSA: hda/realtek: cs35l41: Fixup remaining asus strix models
Sean Christopherson <seanjc(a)google.com>
KVM: nVMX: Fold requested virtual interrupt check into has_nested_events()
Sean Christopherson <seanjc(a)google.com>
KVM: nVMX: Check for pending posted interrupts when looking for nested events
Sean Christopherson <seanjc(a)google.com>
KVM: nVMX: Request immediate exit iff pending nested event needs injection
Sean Christopherson <seanjc(a)google.com>
KVM: nVMX: Add a helper to get highest pending from Posted Interrupt vector
Sean Christopherson <seanjc(a)google.com>
KVM: VMX: Split out the non-virtualization part of vmx_interrupt_blocked()
Gautam Menghani <gautam(a)linux.ibm.com>
KVM: PPC: Book3S HV nestedv2: Add DPDES support in helper library for Guest state buffer
Gautam Menghani <gautam(a)linux.ibm.com>
KVM: PPC: Book3S HV nestedv2: Fix doorbell emulation
Jason Chen <Jason-ch.Chen(a)mediatek.com>
remoteproc: mediatek: Increase MT8188/MT8195 SCP core0 DRAM size
Wentong Wu <wentong.wu(a)intel.com>
media: ivsc: csi: don't count privacy on as error
Ricardo Ribalda <ribalda(a)chromium.org>
media: uvcvideo: Fix integer overflow calculating timestamp
Jan Kara <jack(a)suse.cz>
jbd2: avoid infinite transaction commit loop
Jan Kara <jack(a)suse.cz>
jbd2: precompute number of transaction descriptor blocks
Jan Kara <jack(a)suse.cz>
jbd2: make jbd2_journal_get_max_txn_bufs() internal
Harshit Mogalapalli <harshit.m.mogalapalli(a)oracle.com>
media: imx-pxp: Fix ERR_PTR dereference in pxp_probe()
Tommaso Merciai <tomm.merciai(a)gmail.com>
media: i2c: alvium: Move V4L2_CID_GAIN to V4L2_CID_ANALOG_GAIN
Wentong Wu <wentong.wu(a)intel.com>
media: ivsc: csi: add separate lock for v4l2 control handler
Javier Carrasco <javier.carrasco.cruz(a)gmail.com>
leds: mt6360: Fix memory leak in mt6360_init_isnk_properties()
Thomas Weißschuh <linux(a)weissschuh.net>
leds: triggers: Flush pending brightness before activating trigger
Ofir Gal <ofir.gal(a)volumez.com>
md/md-bitmap: fix writing non bitmap pages
Ilpo Järvinen <ilpo.jarvinen(a)linux.intel.com>
leds: ss4200: Convert PCIBIOS_* return codes to errnos
Jay Buddhabhatti <jay.buddhabhatti(a)amd.com>
drivers: soc: xilinx: check return status of get_api_version()
Javier Carrasco <javier.carrasco.cruz(a)gmail.com>
cpufreq: qcom-nvmem: fix memory leaks in probe error paths
Bitterblue Smith <rtl8821cerfe2(a)gmail.com>
wifi: rtw88: usb: Further limit the TX aggregation
Bitterblue Smith <rtl8821cerfe2(a)gmail.com>
wifi: rtw88: usb: Fix disconnection after beacon loss
Po-Hao Huang <phhuang(a)realtek.com>
wifi: rtw89: fix HW scan not aborting properly
Rafael Beims <rafael.beims(a)toradex.com>
wifi: mwifiex: Fix interface type change
Rafael J. Wysocki <rafael.j.wysocki(a)intel.com>
genirq: Set IRQF_COND_ONESHOT in request_irq()
levi.yun <yeoreum.yun(a)arm.com>
trace/pid_list: Change gfp flags in pid_list_fill_irq()
Pavel Begunkov <asml.silence(a)gmail.com>
io_uring: don't allow netpolling with SETUP_IOPOLL
Pavel Begunkov <asml.silence(a)gmail.com>
io_uring: tighten task exit cancellations
Pavel Begunkov <asml.silence(a)gmail.com>
io_uring: fix lost getsockopt completions
Baokun Li <libaokun1(a)huawei.com>
ext4: make sure the first directory block is not a hole
Baokun Li <libaokun1(a)huawei.com>
ext4: check dot and dotdot of dx_root before making dir indexed
Ming Lei <ming.lei(a)redhat.com>
block: check bio alignment in blk_mq_submit_bio
Paolo Pisati <p.pisati(a)gmail.com>
m68k: amiga: Turn off Warp1260 interrupts during boot
Jan Kara <jack(a)suse.cz>
udf: Avoid using corrupted block bitmap buffer
Frederic Weisbecker <frederic(a)kernel.org>
task_work: Introduce task_work_cancel() again
Frederic Weisbecker <frederic(a)kernel.org>
task_work: s/task_work_cancel()/task_work_cancel_func()/
Steve French <stfrench(a)microsoft.com>
cifs: mount with "unix" mount option for SMB1 incorrectly handled
Steve French <stfrench(a)microsoft.com>
cifs: fix reconnect with SMB1 UNIX Extensions
Steve French <stfrench(a)microsoft.com>
cifs: fix potential null pointer use in destroy_workqueue in init_cifs error path
Fedor Pchelkin <pchelkin(a)ispras.ru>
apparmor: use kvfree_sensitive to free data->data
Sung Joon Kim <sungjoon.kim(a)amd.com>
drm/amd/display: Check for NULL pointer
Shreyas Deodhar <sdeodhar(a)marvell.com>
scsi: qla2xxx: Fix optrom version displayed in FDMI
Alex Deucher <alexander.deucher(a)amd.com>
drm/amd/display: fix corruption with high refresh rates on DCN 3.0
Ma Ke <make24(a)iscas.ac.cn>
drm/gma500: fix null pointer dereference in psb_intel_lvds_get_modes
Ma Ke <make24(a)iscas.ac.cn>
drm/gma500: fix null pointer dereference in cdv_intel_lvds_get_modes
Pavel Begunkov <asml.silence(a)gmail.com>
io_uring/io-wq: limit retrying worker initialisation
Paul Moore <paul(a)paul-moore.com>
lsm: fixup the inode xattr capability handling
Kory Maincent <kory.maincent(a)bootlin.com>
media: i2c: Kconfig: Fix missing firmware upload config select
Jan Kara <jack(a)suse.cz>
ext2: Verify bitmap and itable block numbers before using them
Chao Yu <chao(a)kernel.org>
hfs: fix to initialize fields of hfs_inode_info after hfs_alloc_inode()
Thomas Weißschuh <linux(a)weissschuh.net>
sysctl: always initialize i_uid/i_gid
Igor Pylypiv <ipylypiv(a)google.com>
ata: libata-scsi: Honor the D_SENSE bit for CK_COND=1 and no error
Igor Pylypiv <ipylypiv(a)google.com>
ata: libata-scsi: Do not overwrite valid sense data when CK_COND=1
Dikshita Agarwal <quic_dikshita(a)quicinc.com>
media: venus: fix use after free in vdec_close
Joe Hattori <joe(a)pf.is.s.u-tokyo.ac.jp>
char: tpm: Fix possible memory leak in tpm_bios_measurements_open()
Vitor Soares <vitor.soares(a)toradex.com>
tpm_tis_spi: add missing attpm20p SPI device ID entry
Thomas Weißschuh <linux(a)weissschuh.net>
selftests/nolibc: fix printf format mismatch in expect_str_buf_eq()
Igor Pylypiv <ipylypiv(a)google.com>
ata: libata-scsi: Fix offsets for the fixed format sense data
Damien Le Moal <dlemoal(a)kernel.org>
null_blk: Fix description of the fua parameter
Alain Volmat <alain.volmat(a)foss.st.com>
media: stm32: dcmipp: correct error handling in dcmipp_create_subdevs
Yu Kuai <yukuai3(a)huawei.com>
md/raid5: fix spares errors about rcu usage
Eric Sandeen <sandeen(a)redhat.com>
fuse: verify {g,u}id mount options correctly
Tejun Heo <tj(a)kernel.org>
sched/fair: set_load_weight() must also call reweight_task() for SCHED_IDLE tasks
Zong-Zhe Yang <kevin_yang(a)realtek.com>
wifi: mac80211: chanctx emulation set CHANGE_CHANNEL when in_reconfig
Chuck Lever <chuck.lever(a)oracle.com>
NFSD: Support write delegations in LAYOUTGET
Thomas Hellström <thomas.hellstrom(a)linux.intel.com>
drm/xe: Use write-back caching mode for system memory on DGFX
Nicolas Dichtel <nicolas.dichtel(a)6wind.com>
ipv6: take care of scope when choosing the src addr
Nicolas Dichtel <nicolas.dichtel(a)6wind.com>
ipv4: fix source address selection with route leak
Nicolas Dichtel <nicolas.dichtel(a)6wind.com>
ipv6: fix source address selection with route leak
Pavel Begunkov <asml.silence(a)gmail.com>
kernel: rerun task_work while freezing in get_signal()
Filipe Manana <fdmanana(a)suse.com>
btrfs: fix extent map use-after-free when adding pages to compressed bio
Lai Jiangshan <jiangshan.ljs(a)antgroup.com>
workqueue: Always queue work items to the newest PWQ for order workqueues
Chengen Du <chengen.du(a)canonical.com>
af_packet: Handle outgoing VLAN packets without hardware offloading
Breno Leitao <leitao(a)debian.org>
net: netconsole: Disable target before netpoll cleanup
Yu Liao <liaoyu15(a)huawei.com>
tick/broadcast: Make takeover of broadcast hrtimer reliable
Krzysztof Kozlowski <krzysztof.kozlowski(a)linaro.org>
dt-bindings: thermal: correct thermal zone node name limit
Krzysztof Kozlowski <krzysztof.kozlowski(a)linaro.org>
thermal/drivers/broadcom: Fix race between removal and clock disable
Sungjong Seo <sj1557.seo(a)samsung.com>
exfat: fix potential deadlock on __exfat_get_dentry_set
Takashi Sakamoto <o-takashi(a)sakamocchi.jp>
Revert "firewire: Annotate struct fw_iso_packet with __counted_by()"
Ard Biesheuvel <ardb(a)kernel.org>
x86/efistub: Revert to heap allocated boot_params for PE entrypoint
Ard Biesheuvel <ardb(a)kernel.org>
x86/efistub: Avoid returning EFI_SUCCESS on error
Yu Zhao <yuzhao(a)google.com>
mm/mglru: fix ineffective protection calculation
Yu Zhao <yuzhao(a)google.com>
mm/mglru: fix overshooting shrinker memory
Tetsuo Handa <penguin-kernel(a)I-love.SAKURA.ne.jp>
mm: mmap_lock: replace get_memcg_path_buf() with on-stack buffer
Yu Zhao <yuzhao(a)google.com>
mm/mglru: fix div-by-zero in vmpressure_calc_level()
Miaohe Lin <linmiaohe(a)huawei.com>
mm/hugetlb: fix possible recursive locking detected warning
Aristeu Rozanski <aris(a)redhat.com>
hugetlb: force allocating surplus hugepages on mempolicy allowed nodes
Gavin Shan <gshan(a)redhat.com>
mm/huge_memory: avoid PMD-size page cache if needed
Yang Shi <yang(a)os.amperecomputing.com>
mm: huge_memory: use !CONFIG_64BIT to relax huge page alignment on 32 bit machines
Jann Horn <jannh(a)google.com>
landlock: Don't lose track of restrictions on cred_transfer
Mickaël Salaün <mic(a)digikod.net>
selftests/landlock: Add cred_transfer test
Jason-JH.Lin <jason-jh.lin(a)mediatek.com>
mailbox: mtk-cmdq: Move devm_mbox_controller_register() after devm_pm_runtime_enable()
Peng Fan <peng.fan(a)nxp.com>
mailbox: imx: fix TXDB_V2 channel race condition
Andrew Davis <afd(a)ti.com>
mailbox: omap: Fix mailbox interrupt sharing
Richard Genoud <richard.genoud(a)bootlin.com>
remoteproc: k3-r5: Fix IPC-only mode detection
Nícolas F. R. A. Prado <nfraprado(a)collabora.com>
remoteproc: mediatek: Don't attempt to remap l1tcm memory if missing
Christophe JAILLET <christophe.jaillet(a)wanadoo.fr>
power: supply: ingenic: Fix some error handling paths in ingenic_battery_get_property()
Christophe JAILLET <christophe.jaillet(a)wanadoo.fr>
power: supply: ab8500: Fix error handling when calling iio_read_channel_processed()
Tiezhu Yang <yangtiezhu(a)loongson.cn>
LoongArch: Check TIF_LOAD_WATCH to enable user space watchpoint
Yang Yang <yang.yang(a)vivo.com>
sbitmap: fix io hung due to race on sbitmap_word::cleared
Suren Baghdasaryan <surenb(a)google.com>
alloc_tag: fix page_ext_get/page_ext_put sequence during page splitting
Suren Baghdasaryan <surenb(a)google.com>
lib: reuse page_ext_data() to obtain codetag_ref
Suren Baghdasaryan <surenb(a)google.com>
lib: add missing newline character in the warning message
Carlos López <clopez(a)suse.de>
s390/dasd: fix error checks in dasd_copy_pair_store()
Christophe Leroy <christophe.leroy(a)csgroup.eu>
powerpc/8xx: fix size given to set_huge_pte_at()
Heming Zhao <heming.zhao(a)suse.com>
md-cluster: fix hanging issue while a new disk adding
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Keep runs for $MFT::$ATTR_DATA and $MFT::$ATTR_BITMAP
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Missed error return
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Fix the format of the "nocase" mount option
Csókás, Bence <csokas.bence(a)prolan.hu>
rtc: interface: Add RTC offset to alarm after fix-up
Ryusuke Konishi <konishi.ryusuke(a)gmail.com>
nilfs2: avoid undefined behavior in nilfs_cnt32_ge macro
SeongJae Park <sj(a)kernel.org>
selftests/damon/access_memory: use user-defined region size
David Hildenbrand <david(a)redhat.com>
fs/proc/task_mmu: properly detect PM_MMAP_EXCLUSIVE per page of PMD-mapped THPs
David Hildenbrand <david(a)redhat.com>
fs/proc/task_mmu: don't indicate PM_MMAP_EXCLUSIVE without PM_PRESENT
David Hildenbrand <david(a)redhat.com>
fs/proc/task_mmu: indicate PM_FILE for PMD-mapped file THP
Geert Uytterhoeven <geert+renesas(a)glider.be>
pinctrl: renesas: r8a779g0: Fix TPU suffixes
Geert Uytterhoeven <geert+renesas(a)glider.be>
pinctrl: renesas: r8a779g0: Fix TCLK suffixes
Geert Uytterhoeven <geert+renesas(a)glider.be>
pinctrl: renesas: r8a779g0: FIX PWM suffixes
Geert Uytterhoeven <geert+renesas(a)glider.be>
pinctrl: renesas: r8a779g0: Fix IRQ suffixes
Geert Uytterhoeven <geert+renesas(a)glider.be>
pinctrl: renesas: r8a779g0: Fix (H)SCIF3 suffixes
Geert Uytterhoeven <geert+renesas(a)glider.be>
pinctrl: renesas: r8a779g0: Fix (H)SCIF1 suffixes
Geert Uytterhoeven <geert+renesas(a)glider.be>
pinctrl: renesas: r8a779g0: Fix FXR_TXEN[AB] suffixes
Geert Uytterhoeven <geert+renesas(a)glider.be>
pinctrl: renesas: r8a779g0: Fix CANFD5 suffix
Richard Genoud <richard.genoud(a)bootlin.com>
rtc: tps6594: Fix memleak in probe
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Fix field-spanning write in INDEX_HDR
Andy Shevchenko <andriy.shevchenko(a)linux.intel.com>
fs/ntfs3: Drop stray '\' (backslash) in formatting string
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Correct undo if ntfs_create_inode failed
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Replace inode_trylock with inode_lock
Peng Fan <peng.fan(a)nxp.com>
pinctrl: freescale: mxs: Fix refcount of child
Yang Yingliang <yangyingliang(a)huawei.com>
pinctrl: ti: ti-iodelay: fix possible memory leak when pinctrl_enable() fails
Yang Yingliang <yangyingliang(a)huawei.com>
pinctrl: single: fix possible memory leak when pinctrl_enable() fails
Yang Yingliang <yangyingliang(a)huawei.com>
pinctrl: core: fix possible memory leak when pinctrl_enable() fails
Dmitry Yashin <dmt.yashin(a)gmail.com>
pinctrl: rockchip: update rk3308 iomux routes
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Add missing .dirty_folio in address_space_operations
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Fix getting file type
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Missed NI_FLAG_UPDATE_PARENT setting
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Deny getting attr data block in compressed frame
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Fix transform resident to nonresident for compressed files
Konstantin Komarov <almaz.alexandrovich(a)paragon-software.com>
fs/ntfs3: Merge synonym COMPRESSION_UNIT and NTFS_LZNT_CUNIT
Martin Willi <martin(a)strongswan.org>
net: dsa: b53: Limit chip-wide jumbo frame config to CPU ports
Martin Willi <martin(a)strongswan.org>
net: dsa: mv88e6xxx: Limit chip-wide frame size config to CPU ports
Ido Schimmel <idosch(a)nvidia.com>
ipv4: Fix incorrect TOS in fibmatch route get reply
Ido Schimmel <idosch(a)nvidia.com>
ipv4: Fix incorrect TOS in route get reply
Pablo Neira Ayuso <pablo(a)netfilter.org>
net: flow_dissector: use DEBUG_NET_WARN_ON_ONCE
Joshua Washington <joshwash(a)google.com>
gve: Fix XDP TX completion handling when counters overflow
Chen Hanxiao <chenhx.fnst(a)fujitsu.com>
ipvs: properly dereference pe in ip_vs_add_service
Florian Westphal <fw(a)strlen.de>
netfilter: nf_set_pipapo: fix initial map fill
Pablo Neira Ayuso <pablo(a)netfilter.org>
netfilter: ctnetlink: use helper function to calculate expect ID
Jiaxun Yang <jiaxun.yang(a)flygoat.com>
MIPS: Fix fallback march for SB1
Konstantin Taranov <kotaranov(a)microsoft.com>
RDMA/mana_ib: Set correct device into ib
Konstantin Taranov <kotaranov(a)microsoft.com>
RDMA/mana_ib: set node_guid
Jack Wang <jinpu.wang(a)ionos.com>
bnxt_re: Fix imm_data endianness
David Ahern <dsahern(a)kernel.org>
RDMA: Fix netdev tracker in ib_device_set_netdev
David Gstir <david(a)sigma-star.at>
crypto: mxs-dcp - Ensure payload is zero when using key slot
Jon Pan-Doh <pandoh(a)google.com>
iommu/vt-d: Fix identity map bounds in si_domain_init()
Chengchang Tang <tangchengchang(a)huawei.com>
RDMA/hns: Fix mbx timing out before CMD execution is completed
Chengchang Tang <tangchengchang(a)huawei.com>
RDMA/hns: Fix insufficient extend DB for VFs.
Chengchang Tang <tangchengchang(a)huawei.com>
RDMA/hns: Fix undifined behavior caused by invalid max_sge
Chengchang Tang <tangchengchang(a)huawei.com>
RDMA/hns: Fix shift-out-bounds when max_inline_data is 0
Chengchang Tang <tangchengchang(a)huawei.com>
RDMA/hns: Fix missing pagesize and alignment check in FRMR
Junxian Huang <huangjunxian6(a)hisilicon.com>
RDMA/hns: Fix unmatch exception handling when init eq table fails
Junxian Huang <huangjunxian6(a)hisilicon.com>
RDMA/hns: Fix soft lockup under heavy CEQE load
Junxian Huang <huangjunxian6(a)hisilicon.com>
RDMA/hns: Check atomic wr length
Nick Bowler <nbowler(a)draconx.ca>
macintosh/therm_windtunnel: fix module unload.
Michael Ellerman <mpe(a)ellerman.id.au>
powerpc/xmon: Fix disassembly CPU feature checks
Lu Baolu <baolu.lu(a)linux.intel.com>
iommu/vt-d: Fix aligned pages in calculate_psi_aligned_address()
Lu Baolu <baolu.lu(a)linux.intel.com>
iommu/vt-d: Limit max address mask to MAX_AGAW_PFN_WIDTH
Frank Li <Frank.Li(a)nxp.com>
PCI: dwc: Fix index 0 incorrectly being interpreted as a free ATU slot
Manivannan Sadhasivam <manivannan.sadhasivam(a)linaro.org>
PCI: qcom-ep: Disable resources unconditionally during PERST# assert
Dominique Martinet <dominique.martinet(a)atmark-techno.com>
MIPS: Octeron: remove source file executable bit
Lorenzo Bianconi <lorenzo(a)kernel.org>
clk: en7523: fix rate divider for slic and spi clocks
Stephen Boyd <swboyd(a)chromium.org>
clk: qcom: Park shared RCGs upon registration
Abel Vesa <abel.vesa(a)linaro.org>
clk: qcom: gcc-x1e80100: Set parent rate for USB3 sec and tert PHY pipe clks
Chen Ni <nichen(a)iscas.ac.cn>
clk: qcom: kpss-xcc: Return of_clk_add_hw_provider to transfer the error
Nivas Varadharajan Mugunthakumar <nivasx.varadharajan.mugunthakumar(a)intel.com>
crypto: qat - extend scope of lock in adf_cfg_add_key_value_param()
Heiko Stuebner <heiko.stuebner(a)cherry.de>
nvmem: rockchip-otp: set add_legacy_fixed_of_cells config option
Justin Tee <justin.tee(a)broadcom.com>
scsi: lpfc: Revise lpfc_prep_embed_io routine with proper endian macro usages
Denis Arefev <arefev(a)swemel.ru>
net: missing check virtio
Michael S. Tsirkin <mst(a)redhat.com>
vhost/vsock: always initialize seqpacket_allow
Dan Carpenter <dan.carpenter(a)linaro.org>
PCI: endpoint: Fix error handling in epf_ntb_epc_cleanup()
Dan Carpenter <dan.carpenter(a)linaro.org>
PCI: endpoint: Clean up error handling in vpci_scan_bus()
Georgi Djakov <quic_c_gdjako(a)quicinc.com>
iommu/arm-smmu-qcom: Register the TBU driver in qcom_smmu_impl_init
Aleksandr Mishin <amishin(a)t-argos.ru>
ASoC: amd: Adjust error handling in case of absent codec device
Guenter Roeck <linux(a)roeck-us.net>
eeprom: ee1004: Call i2c_new_scanned_device to instantiate thermal sensor
Christoph Schlameuss <schlameuss(a)linux.ibm.com>
kvm: s390: Reject memory region operations for ucontrol VMs
Benjamin Marzinski <bmarzins(a)redhat.com>
dm-raid: Fix WARN_ON_ONCE check for sync_thread in raid_resume
Abel Vesa <abel.vesa(a)linaro.org>
clk: qcom: gcc-x1e80100: Fix halt_check for all pipe clocks
Dmitry Torokhov <dmitry.torokhov(a)gmail.com>
Input: elan_i2c - do not leave interrupt disabled on suspend failure
Leon Romanovsky <leon(a)kernel.org>
RDMA/device: Return error earlier if port in not valid
Arnd Bergmann <arnd(a)arndb.de>
mtd: make mtd_test.c a separate module
Joao Martins <joao.m.martins(a)oracle.com>
iommufd/iova_bitmap: Check iova_bitmap_done() after set ahead
Joao Martins <joao.m.martins(a)oracle.com>
iommufd/selftest: Fix tests to use MOCK_PAGE_SIZE based buffer sizes
Joao Martins <joao.m.martins(a)oracle.com>
iommufd/selftest: Add tests for <= u8 bitmap sizes
Joao Martins <joao.m.martins(a)oracle.com>
iommufd/selftest: Fix iommufd_test_dirty() to handle <u8 bitmaps
Joao Martins <joao.m.martins(a)oracle.com>
iommufd/selftest: Fix dirty bitmap tests with u8 bitmaps
Chen Ni <nichen(a)iscas.ac.cn>
ASoC: max98088: Check for clk_prepare_enable() error
Nathan Lynch <nathanl(a)linux.ibm.com>
powerpc/prom: Add CPU info to hardware description string later
Harald Freudenberger <freude(a)linux.ibm.com>
hwrng: core - Fix wrong quality calculation at hw rng registration
Huai-Yuan Liu <qq810974084(a)gmail.com>
scsi: lpfc: Fix a possible null pointer dereference
Aleksandr Mishin <amishin(a)t-argos.ru>
ASoC: qcom: Adjust issues in case of DT error in asoc_qcom_lpass_cpu_platform_probe()
Honggang LI <honggangli(a)163.com>
RDMA/rxe: Don't set BTH_ACK_MASK for UC or UD QPs
Or Har-Toov <ohartoov(a)nvidia.com>
RDMA/mlx5: Use sq timestamp as QP timestamp when RoCE is disabled
Leon Romanovsky <leon(a)kernel.org>
RDMA/mlx4: Fix truncated output warning in alias_GUID.c
Leon Romanovsky <leon(a)kernel.org>
RDMA/mlx4: Fix truncated output warning in mad.c
Andrei Lalaev <andrei.lalaev(a)anton-paar.com>
Input: qt1050 - handle CHIP_ID reading error
Konrad Dybcio <konrad.dybcio(a)linaro.org>
interconnect: qcom: qcm2290: Fix mas_snoc_bimc RPM master ID
Taniya Das <quic_tdas(a)quicinc.com>
clk: qcom: gpucc-sa8775p: Update wait_val fields for GPU GDSC's
Taniya Das <quic_tdas(a)quicinc.com>
clk: qcom: gpucc-sa8775p: Park RCG's clk source at XO during disable
Taniya Das <quic_tdas(a)quicinc.com>
clk: qcom: gpucc-sa8775p: Remove the CLK_IS_CRITICAL and ALWAYS_ON flags
Taniya Das <quic_tdas(a)quicinc.com>
clk: qcom: gcc-sa8775p: Update the GDSC wait_val fields and flags
Taniya Das <quic_tdas(a)quicinc.com>
clk: qcom: gpucc-sm8350: Park RCG's clk source at XO during disable
Michael Walle <mwalle(a)kernel.org>
mtd: spi-nor: winbond: fix w25q128 regression
Leon Romanovsky <leon(a)kernel.org>
RDMA/cache: Release GID table even if leak is detected
Hao Ge <gehao(a)kylinos.cn>
ASoc: PCM6240: Return directly after a failed devm_kzalloc() in pcmdevice_i2c_probe()
Neil Armstrong <neil.armstrong(a)linaro.org>
usb: typec-mux: nb7vpq904m: unregister typec switch on probe error and remove
Neil Armstrong <neil.armstrong(a)linaro.org>
usb: typec-mux: ptn36502: unregister typec switch on probe error and remove
Simon Trimmer <simont(a)opensource.cirrus.com>
ASoC: cs35l56: Accept values greater than 0 as IRQ numbers
Shenghao Ding <shenghao-ding(a)ti.com>
ASoc: tas2781: Enable RCA-based playback without DSP firmware download
Sourabh Jain <sourabhjain(a)linux.ibm.com>
powerpc/kexec_file: fix cpus node update to FDT
Chiara Meiohas <cmeiohas(a)nvidia.com>
RDMA/mlx5: Set mkeys for dmabuf at PAGE_SIZE
James Clark <james.clark(a)arm.com>
coresight: Fix ref leak when of_coresight_parse_endpoint() fails
Shivaprasad G Bhat <sbhat(a)linux.ibm.com>
KVM: PPC: Book3S HV: Fix the get_one_reg of SDAR
Shivaprasad G Bhat <sbhat(a)linux.ibm.com>
KVM: PPC: Book3S HV: Fix the set_one_reg for MMCR3
Mostafa Saleh <smostafa(a)google.com>
iommu/arm-smmu-v3: Avoid uninitialized asid in case of error
Nuno Sa <nuno.sa(a)analog.com>
iio: adc: adi-axi-adc: don't allow concurrent enable/disable calls
Antoniu Miclaus <antoniu.miclaus(a)analog.com>
iio: frequency: adrf6780: rm clk provider include
Nuno Sa <nuno.sa(a)analog.com>
iio: adc: ad9467: use DMA safe buffer for spi
Xianwei Zhao <xianwei.zhao(a)amlogic.com>
clk: meson: s4: fix pwm_j_div parent clock
Xianwei Zhao <xianwei.zhao(a)amlogic.com>
clk: meson: s4: fix fixed_pll_dco clock
Taniya Das <quic_tdas(a)quicinc.com>
clk: qcom: camcc-sc7280: Add parent dependency to all camera GDSCs
Taniya Das <quic_tdas(a)quicinc.com>
clk: qcom: gcc-sc7280: Update force mem core bit for UFS ICE clock
Lothar Rubusch <l.rubusch(a)gmail.com>
crypto: atmel-sha204a - fix negated return value
Christophe JAILLET <christophe.jaillet(a)wanadoo.fr>
crypto: tegra - Remove an incorrect iommu_fwspec_free() call in tegra_se_remove()
Minwoo Im <minwoo.im(a)samsung.com>
scsi: ufs: mcq: Fix missing argument 'hba' in MCQ_OPR_OFFSET_n
Andy Chiu <andy.chiu(a)sifive.com>
riscv: smp: fail booting up smp if inconsistent vlen is detected
Jon Hunter <jonathanh(a)nvidia.com>
PCI: tegra194: Set EP alignment restriction for inbound ATU
Marek Vasut <marek.vasut+renesas(a)mailbox.org>
PCI: rcar: Demote WARN() to dev_warn_ratelimited() in rcar_pcie_wakeup()
Aleksandr Mishin <amishin(a)t-argos.ru>
PCI: keystone: Fix NULL pointer dereference in case of DT error in ks_pcie_setup_rc_app_regs()
Siddharth Vadapalli <s-vadapalli(a)ti.com>
PCI: keystone: Don't enable BAR 0 for AM654x
Siddharth Vadapalli <s-vadapalli(a)ti.com>
PCI: keystone: Relocate ks_pcie_set/clear_dbi_mode()
Ilpo Järvinen <ilpo.jarvinen(a)linux.intel.com>
PCI: Fix resource double counting on remove & rescan
Manivannan Sadhasivam <manivannan.sadhasivam(a)linaro.org>
PCI: endpoint: pci-epf-test: Make use of cached 'epc_features' in pci_epf_test_core_init()
Chenyuan Yang <chenyuan0y(a)gmail.com>
iio: Fix the sorting functionality in iio_gts_build_avail_time_table
Benjamin Coddington <bcodding(a)redhat.com>
SUNRPC: Fixup gss_status tracepoint error output
Christoph Hellwig <hch(a)lst.de>
nfs: pass explicit offset/count to trace events
Luke D. Jones <luke(a)ljones.dev>
platform/x86: asus-wmi: fix TUF laptop RGB variant
Ian Rogers <irogers(a)google.com>
perf dso: Fix address sanitizer build
Andreas Larsson <andreas(a)gaisler.com>
sparc64: Fix incorrect function signature and add prototype for prom_cif_init
Dan Carpenter <dan.carpenter(a)linaro.org>
leds: flash: leds-qcom-flash: Test the correct variable in init
Thomas Zimmermann <tzimmermann(a)suse.de>
drm/qxl: Pin buffer objects for internal mappings
Jan Kara <jack(a)suse.cz>
ext4: avoid writing unitialized memory to disk in EA inodes
Luis Henriques (SUSE) <luis.henriques(a)linux.dev>
ext4: don't track ranges in fast_commit if inode has inlined data
Olga Kornievskaia <kolga(a)netapp.com>
NFSv4.1 another fix for EXCHGID4_FLAG_USE_PNFS_DS for DS server
NeilBrown <neilb(a)suse.de>
SUNRPC: avoid soft lockup when transmitting UDP to reachable server.
Chuck Lever <chuck.lever(a)oracle.com>
xprtrdma: Fix rpcrdma_reqs_reset()
Javier Carrasco <javier.carrasco.cruz(a)gmail.com>
mfd: omap-usb-tll: Use struct_size to allocate tll
Arnd Bergmann <arnd(a)arndb.de>
mfd: rsmu: Split core code into separate module
Steven Price <steven.price(a)arm.com>
drm/panthor: Record devfreq busy as soon as a job is started
Adrian Hunter <adrian.hunter(a)intel.com>
perf intel-pt: Fix exclude_guest setting
Adrian Hunter <adrian.hunter(a)intel.com>
perf intel-pt: Fix aux_watermark calculation for 64-bit size
Dikshita Agarwal <quic_dikshita(a)quicinc.com>
media: venus: flush all buffers in output plane streamoff
Namhyung Kim <namhyung(a)kernel.org>
perf stat: Fix a segfault with --per-cluster --metric-only
Michael Walle <mwalle(a)kernel.org>
drm/mediatek/dp: Fix spurious kfree()
Michael Walle <mwalle(a)kernel.org>
drm/mediatek: dpi/dsi: Fix possible_crtcs calculation
James Clark <james.clark(a)arm.com>
perf pmu: Restore full PMU name wildcard support
Ian Rogers <irogers(a)google.com>
perf tests: Add some pmu core functionality tests
Ma Ke <make24(a)iscas.ac.cn>
drm/amd/display: Add null check before access structs
Luis Henriques (SUSE) <luis.henriques(a)linux.dev>
ext4: fix infinite loop when replaying fast_commit
Hsiao Chien Sung <shawn.sung(a)mediatek.com>
drm/mediatek: Remove less-than-zero comparison of an unsigned value
Geert Uytterhoeven <geert+renesas(a)glider.be>
drm/panic: Do not select DRM_KMS_HELPER
Jocelyn Falempe <jfalempe(a)redhat.com>
drm/panic: depends on !VT_CONSOLE
Luca Ceresoli <luca.ceresoli(a)bootlin.com>
Revert "leds: led-core: Fix refcount leak in of_led_get()"
Anjelique Melendez <quic_amelende(a)quicinc.com>
leds: rgb: leds-qcom-lpg: Add PPG check for setting/clearing PBS triggers
Chen Ni <nichen(a)iscas.ac.cn>
drm/qxl: Add check for drm_cvt_mode
Lucas Stach <l.stach(a)pengutronix.de>
drm/etnaviv: fix DMA direction handling for cached RW buffers
Namhyung Kim <namhyung(a)kernel.org>
perf report: Fix condition in sort__sym_cmp()
Junhao He <hejunhao3(a)huawei.com>
perf pmus: Fixes always false when compare duplicates aliases
Athira Rajeev <atrajeev(a)linux.vnet.ibm.com>
tools/perf: Fix the string match for "/tmp/perf-$PID.map" files in dso__load
James Clark <james.clark(a)arm.com>
perf test: Make test_arm_callgraph_fp.sh more robust
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
platform/arm64: build drivers even on non-ARM64 platforms
Geert Uytterhoeven <geert+renesas(a)glider.be>
drm/panic: Fix off-by-one logo size checks
Jocelyn Falempe <jfalempe(a)redhat.com>
drm/panic: only draw the foreground color in drm_panic_blit()
Karolina Stolarek <karolina.stolarek(a)intel.com>
drm/ttm/tests: Fix a warning in ttm_bo_unreserve_bulk
Abhinav Kumar <quic_abhinavk(a)quicinc.com>
drm/msm/dpu: drop validity checks for clear_pending_flush() ctl op
Jonathan Marek <jonathan(a)marek.ca>
drm/msm/dsi: set VIDEO_COMPRESSION_MODE_CTRL_WC
Jonathan Marek <jonathan(a)marek.ca>
drm/msm/dsi: set video mode widebus enable bit when widebus is enabled
Hans de Goede <hdegoede(a)redhat.com>
leds: trigger: Unregister sysfs attributes before calling deactivate()
Ming Qian <ming.qian(a)nxp.com>
media: imx-jpeg: Drop initial source change event if capture has been setup
Konrad Dybcio <konrad.dybcio(a)linaro.org>
drm/msm/a6xx: Fix A702 UBWC mode
Abhinav Kumar <quic_abhinavk(a)quicinc.com>
drm/msm/a6xx: use __unused__ to fix compiler warnings for gen7_* includes
Hsiao Chien Sung <shawn.sung(a)mediatek.com>
drm/mediatek: Set DRM mode configs accordingly
Hsiao Chien Sung <shawn.sung(a)mediatek.com>
drm/mediatek: Add DRM_MODE_ROTATE_0 to rotation property
Hsiao Chien Sung <shawn.sung(a)mediatek.com>
drm/mediatek: Add OVL compatible name for MT8195
Hsiao Chien Sung <shawn.sung(a)mediatek.com>
drm/mediatek: Turn off the layers with zero width or height
Hsiao Chien Sung <shawn.sung(a)mediatek.com>
drm/mediatek: Fix destination alpha error in OVL
Hsiao Chien Sung <shawn.sung(a)mediatek.com>
drm/mediatek: Fix XRGB setting error in Mixer
Hsiao Chien Sung <shawn.sung(a)mediatek.com>
drm/mediatek: Fix XRGB setting error in OVL
Hsiao Chien Sung <shawn.sung(a)mediatek.com>
drm/mediatek: Use 8-bit alpha in ETHDR
Hsiao Chien Sung <shawn.sung(a)mediatek.com>
drm/mediatek: Add missing plane settings when async update
Sebastian Andrzej Siewior <bigeasy(a)linutronix.de>
drm/ttm/tests: Let ttm_bo_test consider different ww_mutex implementation.
Laurent Pinchart <laurent.pinchart+renesas(a)ideasonboard.com>
media: renesas: vsp1: Store RPF partition configuration per RPF instance
Laurent Pinchart <laurent.pinchart+renesas(a)ideasonboard.com>
media: renesas: vsp1: Fix _irqsave and _irq mix
Jacopo Mondi <jacopo.mondi(a)ideasonboard.com>
media: rcar-csi2: Cleanup subdevice in remove()
Jacopo Mondi <jacopo.mondi(a)ideasonboard.com>
media: rcar-csi2: Disable runtime_pm in probe error
Jacopo Mondi <jacopo.mondi(a)ideasonboard.com>
media: rcar-vin: Fix YUYV8_1X16 handling for CSI-2
Jouni Högander <jouni.hogander(a)intel.com>
drm/i915/psr: Set SU area width as pipe src width
Sean Anderson <sean.anderson(a)linux.dev>
drm: zynqmp_kms: Fix AUX bus not getting unregistered
Christophe JAILLET <christophe.jaillet(a)wanadoo.fr>
drm: zynqmp_dpsub: Fix an error handling path in zynqmp_dpsub_probe()
Daniel Schaefer <dhs(a)frame.work>
media: uvcvideo: Override default flags
Oleksandr Natalenko <oleksandr(a)natalenko.name>
media: uvcvideo: Add quirk for invalid dev_sof in Logitech C920
Ricardo Ribalda <ribalda(a)chromium.org>
media: uvcvideo: Quirk for invalid dev_sof in Logitech C922
Conor Dooley <conor.dooley(a)microchip.com>
media: i2c: imx219: fix msr access command sequence
Ricardo Ribalda <ribalda(a)chromium.org>
media: c8sectpfe: Add missing parameter names
Aleksandr Burakov <a.burakov(a)rosalinux.ru>
saa7134: Unchecked i2c_transfer function result fixed
Alex Deucher <alexander.deucher(a)amd.com>
drm/amd/display: use pre-allocated temp structure for bounding box
Dan Carpenter <dan.carpenter(a)linaro.org>
ipmi: ssif_bmc: prevent integer overflow on 32bit systems
Jiri Olsa <jolsa(a)kernel.org>
x86/shstk: Make return uprobe work with shadow stack
Jouni Högander <jouni.hogander(a)intel.com>
drm/i915/psr: Print Panel Replay status instead of frame lock status
Jouni Högander <jouni.hogander(a)intel.com>
drm/i915/display: Skip Panel Replay on pipe comparison if no active planes
Adam Ford <aford173(a)gmail.com>
drm/bridge: samsung-dsim: Set P divider based on min/max of fin pll
Yunfei Dong <yunfei.dong(a)mediatek.com>
media: mediatek: vcodec: Fix unreasonable data conversion
Irui Wang <irui.wang(a)mediatek.com>
media: mediatek: vcodec: Handle invalid decoder vsi
Ian Rogers <irogers(a)google.com>
perf maps: Fix use after free in __maps__fixup_overlap_and_insert
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
drm/msm/dp: fix runtime_pm handling in dp_wait_hpd_asserted
Junhao Xie <bigfoot(a)classfun.cn>
drm/msm/dpu: drop duplicate drm formats from wb2_formats arrays
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
Revert "drm/msm/dpu: drop dpu_encoder_phys_ops.atomic_mode_set"
Barnabás Czémán <trabarni(a)gmail.com>
drm/msm/dpu: fix encoder irq wait skip
David Hildenbrand <david(a)redhat.com>
s390/uv: Don't call folio_wait_writeback() without a folio reference
Srinivasan Shanmugam <srinivasan.shanmugam(a)amd.com>
drm/amdgpu: Fix type mismatch in amdgpu_gfx_kiq_init_ring
ChiYuan Huang <cy_huang(a)richtek.com>
media: v4l: async: Fix NULL pointer dereference in adding ancillary links
Ricardo Ribalda <ribalda(a)chromium.org>
media: i2c: hi846: Fix V4L2_SUBDEV_FORMAT_TRY get_selection()
Bryan O'Donoghue <bryan.odonoghue(a)linaro.org>
media: i2c: Fix imx412 exposure control
Jouni Högander <jouni.hogander(a)intel.com>
drm/i915/psr: Use enable boolean from intel_crtc_state for Early Transport
Ricardo Ribalda <ribalda(a)chromium.org>
media: imon: Fix race getting ictx->lock
Zheng Yejian <zhengyejian1(a)huawei.com>
media: dvb-usb: Fix unexpected infinite loop in dvb_usb_read_remote_control()
Mikhail Kobuk <m.kobuk(a)ispras.ru>
media: pci: ivtv: Add check for DMA map result
Arnd Bergmann <arnd(a)arndb.de>
drm/amd/display: Move 'struct scaler_data' off stack
Arnd Bergmann <arnd(a)arndb.de>
drm/amd/display: fix graphics_object_id size
Arnd Bergmann <arnd(a)arndb.de>
drm/amd/display: dynamically allocate dml2_configuration_options structures
Srinivasan Shanmugam <srinivasan.shanmugam(a)amd.com>
drm/amdgpu: Fix snprintf usage in amdgpu_gfx_kiq_init_ring
Kuro Chung <kuro.chung(a)ite.com.tw>
drm/bridge: it6505: fix hibernate to resume no display issue
Douglas Anderson <dianders(a)chromium.org>
drm/panel: ilitek-ili9882t: Check for errors on the NOP in prepare()
Douglas Anderson <dianders(a)chromium.org>
drm/panel: ilitek-ili9882t: If prepare fails, disable GPIO before regulators
Douglas Anderson <dianders(a)chromium.org>
drm/panel: boe-tv101wum-nl6: Check for errors on the NOP in prepare()
Douglas Anderson <dianders(a)chromium.org>
drm/panel: boe-tv101wum-nl6: If prepare fails, disable GPIO before regulators
Douglas Anderson <dianders(a)chromium.org>
drm/panel: himax-hx8394: Handle errors from mipi_dsi_dcs_set_display_on() better
Tim Van Patten <timvp(a)google.com>
drm/amdgpu: Remove GC HW IP 9.3.0 from noretry=1
Friedrich Vock <friedrich.vock(a)gmx.de>
drm/amdgpu: Check if NBIO funcs are NULL in amdgpu_device_baco_exit
Lijo Lazar <lijo.lazar(a)amd.com>
drm/amdgpu: Fix memory range calculation
Lijo Lazar <lijo.lazar(a)amd.com>
drm/amd/pm: Fix aldebaran pcie speed reporting
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
drm/panel: lg-sw43408: add missing error handling
Douglas Anderson <dianders(a)chromium.org>
drm/mipi-dsi: Fix theoretical int overflow in mipi_dsi_generic_write_seq()
Douglas Anderson <dianders(a)chromium.org>
drm/mipi-dsi: Fix theoretical int overflow in mipi_dsi_dcs_write_seq()
Jouni Högander <jouni.hogander(a)intel.com>
drm/i915/display: Do not print "psr: enabled" for on Panel Replay
Jouni Högander <jouni.hogander(a)intel.com>
drm/i915/psr: Rename has_psr2 as has_sel_update
Mukul Joshi <mukul.joshi(a)amd.com>
drm/amdkfd: Fix CU Masking for GFX 9.4.3
Faiz Abbas <faiz.abbas(a)arm.com>
drm/arm/komeda: Fix komeda probe failing if there are no links in the secondary pipeline
Andy Yan <andy.yan(a)rock-chips.com>
drm/rockchip: vop2: Fix the port mux of VP2
Kuniyuki Iwashima <kuniyu(a)amazon.com>
tcp: Don't access uninit tcp_rsk(req)->ao_keyid in tcp_create_openreq_child().
Luiz Augusto von Dentz <luiz.von.dentz(a)intel.com>
Bluetooth: Fix usage of __hci_cmd_sync_status
Elliot Ayrey <elliot.ayrey(a)alliedtelesis.co.nz>
net: bridge: mst: Check vlan state for egress decision
Taehee Yoo <ap420073(a)gmail.com>
xdp: fix invalid wait context of page_pool_destroy()
Breno Leitao <leitao(a)debian.org>
virtio_net: Fix napi_skb_cache_put warning
Jiri Pirko <jiri(a)resnulli.us>
virtio_net: add support for Byte Queue Limits
Dmitry Antipov <dmantipov(a)yandex.ru>
Bluetooth: hci_core, hci_sync: cleanup struct discovery_state
Iulia Tanasescu <iulia.tanasescu(a)nxp.com>
Bluetooth: hci_event: Set QoS encryption from BIGInfo report
Neeraj Sanjay Kale <neeraj.sanjaykale(a)nxp.com>
Bluetooth: btnxpuart: Add handling for boot-signature timeout errors
Kiran K <kiran.k(a)intel.com>
Bluetooth: btintel_pcie: Fix irq leak
Kiran K <kiran.k(a)intel.com>
Bluetooth: btintel: Refactor btintel_set_ppag()
Sven Peter <sven(a)svenpeter.dev>
Bluetooth: hci_bcm4377: Use correct unit for timeouts
Amit Cohen <amcohen(a)nvidia.com>
selftests: forwarding: devlink_lib: Wait for udev events after reloading
Kory Maincent <kory.maincent(a)bootlin.com>
net: ethtool: pse-pd: Fix possible null-deref
Kory Maincent <kory.maincent(a)bootlin.com>
net: pse-pd: Do not return EOPNOSUPP if config is null
Tengda Wu <wutengda(a)huaweicloud.com>
bpf: Fix null pointer dereference in resolve_prog_type() for BPF_PROG_TYPE_EXT
Jeff Layton <jlayton(a)kernel.org>
nfsd: nfsd_file_lease_notifier_call gets a file_lease as an argument
Shung-Hsi Yu <shung-hsi.yu(a)suse.com>
bpf: fix overflow check in adjust_jmp_off()
Alan Maguire <alan.maguire(a)oracle.com>
bpf: Eliminate remaining "make W=1" warnings in kernel/bpf/btf.o
Alexey Kodanev <aleksei.kodanev(a)bell-sw.com>
bna: adjust 'name' buf size of bna_tcb and bna_ccb structures
Alan Maguire <alan.maguire(a)oracle.com>
bpf: annotate BTF show functions with __printf
Ilpo Järvinen <ilpo.jarvinen(a)linux.intel.com>
selftests/resctrl: Fix closing IMC fds on error and open-code R+W instead of loops
Puranjay Mohan <puranjay(a)kernel.org>
bpf, arm64: Fix trampoline for BPF_TRAMP_F_CALL_ORIG
Geliang Tang <geliang(a)kernel.org>
selftests/bpf: Close obj in error path in xdp_adjust_tail
Geliang Tang <geliang(a)kernel.org>
selftests/bpf: Null checks for links in bpf_tcp_ca
Geliang Tang <geliang(a)kernel.org>
selftests/bpf: Close fd in error path in drop_on_reuseport
John Stultz <jstultz(a)google.com>
locking/rwsem: Add __always_inline annotation to __down_write_common() and inlined callers
Johannes Berg <johannes.berg(a)intel.com>
wifi: virt_wifi: don't use strlen() in const context
Johannes Berg <johannes.berg(a)intel.com>
net: page_pool: fix warning code
Gaosheng Cui <cuigaosheng1(a)huawei.com>
gss_krb5: Fix the error handling path for crypto_sync_skcipher_setkey
Chuck Lever <chuck.lever(a)oracle.com>
NFSD: Fix nfsdcld warning
Benjamin Tissoires <bentiss(a)kernel.org>
bpf: helpers: fix bpf_wq_set_callback_impl signature
En-Wei Wu <en-wei.wu(a)canonical.com>
wifi: virt_wifi: avoid reporting connection success with wrong SSID
Jianbo Liu <jianbol(a)nvidia.com>
xfrm: call xfrm_dev_policy_delete when kill policy
Jianbo Liu <jianbol(a)nvidia.com>
xfrm: fix netdev reference count imbalance
Aleksandr Mishin <amishin(a)t-argos.ru>
wifi: rtw89: Fix array index mistake in rtw89_sta_info_get_iter()
Sandipan Das <sandipan.das(a)amd.com>
perf/x86/amd/uncore: Fix DF and UMC domain identification
Sandipan Das <sandipan.das(a)amd.com>
perf/x86/amd/uncore: Avoid PMU registration if counters are unavailable
Zhang Rui <rui.zhang(a)intel.com>
perf/x86/intel/cstate: Fix Alderlake/Raptorlake/Meteorlake
Adrian Hunter <adrian.hunter(a)intel.com>
perf: Fix default aux_watermark calculation
Adrian Hunter <adrian.hunter(a)intel.com>
perf: Prevent passing zero nr_pages to rb_alloc_aux()
Adrian Hunter <adrian.hunter(a)intel.com>
perf: Fix perf_aux_size() for greater-than 32-bit size
Adrian Hunter <adrian.hunter(a)intel.com>
perf/x86/intel/pt: Fix pt_topa_entry_for_page() address calculation
Ilya Leoshkevich <iii(a)linux.ibm.com>
bpf: Fix atomic probe zero-extension
Tao Chen <chen.dylane(a)gmail.com>
bpftool: Mount bpffs when pinmaps path not under the bpffs
Pu Lehui <pulehui(a)huawei.com>
riscv, bpf: Fix out-of-bounds issue when preparing trampoline image
Steffen Klassert <steffen.klassert(a)secunet.com>
xfrm: Export symbol xfrm_dev_state_delete.
Martin Kaistra <martin.kaistra(a)linutronix.de>
wifi: rtl8xxxu: 8188f: Limit TX power index
Kuan-Chung Chen <damon.chen(a)realtek.com>
wifi: rtw89: 8852b: fix definition of KIP register number
Chih-Kang Chang <gary.chang(a)realtek.com>
wifi: rtw89: wow: fix GTK offload H2C skbuff issue
Karthikeyan Periyasamy <quic_periyasa(a)quicinc.com>
wifi: ath12k: fix peer metadata parsing
Aloka Dixit <quic_alokad(a)quicinc.com>
wifi: ath12k: advertise driver capabilities for MBSSID and EMA
Johannes Berg <johannes.berg(a)intel.com>
wifi: iwlwifi: mvm: always unblock EMLSR on ROC end
Daniel Gabay <daniel.gabay(a)intel.com>
wifi: iwlwifi: fix iwl_mvm_get_valid_rx_ant()
Johannes Berg <johannes.berg(a)intel.com>
wifi: mac80211: correcty limit wider BW TDLS STAs
Johannes Berg <johannes.berg(a)intel.com>
wifi: mac80211: add ieee80211_tdls_sta_link_id()
Pablo Neira Ayuso <pablo(a)netfilter.org>
netfilter: nf_tables: rise cap on SELinux secmark context
Ismael Luceno <iluceno(a)suse.de>
ipvs: Avoid unnecessary calls to skb_is_gso_sctp
Steffen Klassert <steffen.klassert(a)secunet.com>
xfrm: Fix unregister netdevice hang on hardware offload.
Antoine Tenart <atenart(a)kernel.org>
libbpf: Skip base btf sanity checks
Donglin Peng <dolinux.peng(a)gmail.com>
libbpf: Checking the btf_type kind when fixing variable offsets
Jiri Olsa <jolsa(a)kernel.org>
bpf: Change bpf_session_cookie return value to __u64 *
Lukasz Majewski <lukma(a)denx.de>
net: dsa: ksz_common: Allow only up to two HSR HW offloaded ports for KSZ9477
Csókás, Bence <csokas.bence(a)prolan.hu>
net: fec: Fix FEC_ECR_EN1588 being cleared on link-down
Jan Kara <jack(a)suse.cz>
udf: Fix bogus checksum computation in udf_rename()
Antony Antony <antony.antony(a)secunet.com>
xfrm: Log input direction mismatch error in one place
Antony Antony <antony.antony(a)secunet.com>
xfrm: Fix input error path memory access
Daniel Xu <dxu(a)dxuuu.xyz>
bpf: Make bpf_session_cookie() kfunc return long *
Johannes Berg <johannes.berg(a)intel.com>
wifi: iwlwifi: mvm: separate non-BSS/ROC EMLSR blocking
Miri Korenblit <miriam.rachel.korenblit(a)intel.com>
wifi: iwlwifi: mvm: fix re-enabling EMLSR
Johannes Berg <johannes.berg(a)intel.com>
wifi: nl80211: expose can-monitor channel property
Baochen Qiang <quic_bqiang(a)quicinc.com>
wifi: cfg80211: handle 2x996 RU allocation in cfg80211_calculate_bitrate_he()
Baochen Qiang <quic_bqiang(a)quicinc.com>
wifi: cfg80211: fix typo in cfg80211_calculate_bitrate_he()
Aditya Kumar Singh <quic_adisi(a)quicinc.com>
wifi: ath12k: fix per pdev debugfs registration
Baochen Qiang <quic_bqiang(a)quicinc.com>
wifi: ath11k: fix wrong handling of CCMP256 and GCMP ciphers
Baochen Qiang <quic_bqiang(a)quicinc.com>
wifi: ath12k: fix ACPI warning when resume
Thomas Gleixner <tglx(a)linutronix.de>
jump_label: Fix concurrency issues in static_key_slow_dec()
Thomas Gleixner <tglx(a)linutronix.de>
perf/x86: Serialize set_attr_rdpmc()
Ido Schimmel <idosch(a)nvidia.com>
mlxsw: spectrum_acl: Fix ACL scale regression and firmware errors
Ido Schimmel <idosch(a)nvidia.com>
mlxsw: spectrum_acl_erp: Fix object nesting warning
Ido Schimmel <idosch(a)nvidia.com>
lib: objagg: Fix general protection fault
Sean Christopherson <seanjc(a)google.com>
sched/core: Drop spinlocks on contention iff kernel is preemptible
Sean Christopherson <seanjc(a)google.com>
sched/core: Move preempt_model_*() helpers from sched.h to preempt.h
Jan Kara <jack(a)suse.cz>
udf: Fix lock ordering in udf_evict_inode()
Geliang Tang <geliang(a)kernel.org>
selftests/bpf: Check length of recv in test_sockmap
Guangguan Wang <guangguan.wang(a)linux.alibaba.com>
net/smc: set rmb's SG_MAX_SINGLE_ALLOC limitation only when CONFIG_ARCH_NO_SG_CHAIN is defined
Andrii Nakryiko <andrii(a)kernel.org>
libbpf: keep FD_CLOEXEC flag when dup()'ing FD
Arnd Bergmann <arnd(a)arndb.de>
hns3: avoid linking objects into multiple modules
Eric Dumazet <edumazet(a)google.com>
tcp: fix races in tcp_v[46]_err()
Eric Dumazet <edumazet(a)google.com>
tcp: fix races in tcp_abort()
Eric Dumazet <edumazet(a)google.com>
tcp: fix race in tcp_write_err()
Eric Dumazet <edumazet(a)google.com>
tcp: add tcp_done_with_error() helper
Linus Walleij <linus.walleij(a)linaro.org>
net: ethernet: cortina: Restore TSO support
Baochen Qiang <quic_bqiang(a)quicinc.com>
wifi: ath12k: fix wrong definition of CE ring's base address
Baochen Qiang <quic_bqiang(a)quicinc.com>
wifi: ath11k: fix wrong definition of CE ring's base address
Ping-Ke Shih <pkshih(a)realtek.com>
wifi: rtw89: 8852c: correct logic and restore PCI PHY EQ after device resume
P Praneesh <quic_ppranees(a)quicinc.com>
wifi: ath12k: fix firmware crash during reo reinject
P Praneesh <quic_ppranees(a)quicinc.com>
wifi: ath12k: fix invalid memory access while processing fragmented packets
P Praneesh <quic_ppranees(a)quicinc.com>
wifi: ath12k: change DMA direction while mapping reinjected packets
Baochen Qiang <quic_bqiang(a)quicinc.com>
wifi: ath11k: restore country code during resume
Baochen Qiang <quic_bqiang(a)quicinc.com>
wifi: ath11k: refactor setting country code logic
Johannes Berg <johannes.berg(a)intel.com>
wifi: mac80211: reset negotiated TTLM on disconnect
Johannes Berg <johannes.berg(a)intel.com>
wifi: mac80211: cancel TTLM teardown work earlier
Johannes Berg <johannes.berg(a)intel.com>
wifi: mac80211: cancel multi-link reconf work on disconnect
Johannes Berg <johannes.berg(a)intel.com>
wifi: mac80211: fix TTLM teardown work
Miri Korenblit <miriam.rachel.korenblit(a)intel.com>
wifi: iwlwifi: mvm: don't skip link selection
Hagar Hemdan <hagarhem(a)amazon.com>
net: esp: cleanup esp_output_tail_tcp() in case of unsupported ESPINTCP
Ping-Ke Shih <pkshih(a)realtek.com>
wifi: rtw89: 8852b: restore setting for RFE type 5 after device resume
Geliang Tang <geliang(a)kernel.org>
selftests/bpf: Fix prog numbers in test_sockmap
Ivan Babrou <ivan(a)cloudflare.com>
bpftool: Un-const bpf_func_info to fix it for llvm 17 and newer
Baochen Qiang <quic_bqiang(a)quicinc.com>
wifi: ath12k: fix Smatch warnings on ath12k_core_suspend()
Nithyanantham Paramasivam <quic_nithp(a)quicinc.com>
wifi: ath12k: Fix tx completion ring (WBM2SW) setup failure
Pradeep Kumar Chitrapu <quic_pradeepc(a)quicinc.com>
wifi: ath12k: Correct 6 GHz frequency value in rx status
Samasth Norway Ananda <samasth.norway.ananda(a)oracle.com>
wifi: brcmsmac: LCN PHY code is used for BCM4313 2G-only device
Kang Yang <quic_kangyang(a)quicinc.com>
wifi: ath12k: avoid duplicated vdev stop
Karthikeyan Kathirvel <quic_kathirve(a)quicinc.com>
wifi: ath12k: drop failed transmitted frames from metric calculation.
Sven Eckelmann <sven(a)narfation.org>
wifi: ath12k: Don't drop tx_status in failure case
Marek Behún <kabel(a)kernel.org>
firmware: turris-mox-rwtm: Initialize completion before mailbox
Marek Behún <kabel(a)kernel.org>
firmware: turris-mox-rwtm: Fix checking return value of wait_for_completion_timeout()
Marek Behún <kabel(a)kernel.org>
firmware: turris-mox-rwtm: Do not complete if there are no waiters
Christophe Leroy <christophe.leroy(a)csgroup.eu>
vmlinux.lds.h: catch .bss..L* sections into BSS")
Tom Lendacky <thomas.lendacky(a)amd.com>
x86/sev: Do RMP memory coverage check after max_pfn has been set
Yanjun Yang <yangyj.ee(a)gmail.com>
ARM: Remove address checking for MMUless devices
Dmitry Torokhov <dmitry.torokhov(a)gmail.com>
ARM: spitz: fix GPIO assignment for backlight
Thorsten Blum <thorsten.blum(a)toblux.com>
m68k: cmpxchg: Fix return value for default case in __arch_xchg()
Dhananjay Ugwekar <Dhananjay.Ugwekar(a)amd.com>
cpufreq/amd-pstate: Fix the scaling_max_freq setting on shared memory CPPC systems
Dhananjay Ugwekar <Dhananjay.Ugwekar(a)amd.com>
cpufreq/amd-pstate-ut: Convert nominal_freq to khz during comparisons
Luca Weiss <luca.weiss(a)fairphone.com>
arm64: dts: qcom: sm6350: Add missing qcom,non-secure-domain property
Chukun Pan <amadeus(a)jmu.edu.cn>
arm64: dts: rockchip: fixes PHY reset for Lunzn Fastrhino R68S
Chukun Pan <amadeus(a)jmu.edu.cn>
arm64: dts: rockchip: disable display subsystem for Lunzn Fastrhino R6xS
Chukun Pan <amadeus(a)jmu.edu.cn>
arm64: dts: rockchip: remove unused usb2 nodes for Lunzn Fastrhino R6xS
Chukun Pan <amadeus(a)jmu.edu.cn>
arm64: dts: rockchip: fix pmu_io supply for Lunzn Fastrhino R6xS
Chukun Pan <amadeus(a)jmu.edu.cn>
arm64: dts: rockchip: fix usb regulator for Lunzn Fastrhino R6xS
Chukun Pan <amadeus(a)jmu.edu.cn>
arm64: dts: rockchip: fix regulator name for Lunzn Fastrhino R6xS
Cristian Ciocaltea <cristian.ciocaltea(a)collabora.com>
arm64: dts: rockchip: Add missing power-domains for rk356x vop_mmu
Dang Huynh <danct12(a)riseup.net>
arm64: dts: qcom: qrb4210-rb2: Correct max current draw for VBUS
Chen Ni <nichen(a)iscas.ac.cn>
x86/xen: Convert comma to semicolon
Abel Vesa <abel.vesa(a)linaro.org>
arm64: dts: qcom: x1e80100: Fix USB HS PHY 0.8V supply
Adam Ford <aford173(a)gmail.com>
arm64: dts: imx8mp: Fix pgc vpu locations
Adam Ford <aford173(a)gmail.com>
arm64: dts: imx8mp: Fix pgc_mlmix location
Eero Tamminen <oak(a)helsinkinet.fi>
m68k: atari: Fix TT bootup freeze / unexpected (SCU) interrupt messages
Geert Uytterhoeven <geert+renesas(a)glider.be>
arm64: dts: renesas: r9a08g045: Add missing hypervisor virtual timer IRQ
Geert Uytterhoeven <geert+renesas(a)glider.be>
arm64: dts: renesas: r9a07g054: Add missing hypervisor virtual timer IRQ
Geert Uytterhoeven <geert+renesas(a)glider.be>
arm64: dts: renesas: r9a07g044: Add missing hypervisor virtual timer IRQ
Geert Uytterhoeven <geert+renesas(a)glider.be>
arm64: dts: renesas: r9a07g043u: Add missing hypervisor virtual timer IRQ
Geert Uytterhoeven <geert+renesas(a)glider.be>
arm64: dts: renesas: r8a779g0: Add missing hypervisor virtual timer IRQ
Geert Uytterhoeven <geert+renesas(a)glider.be>
arm64: dts: renesas: r8a779f0: Add missing hypervisor virtual timer IRQ
Geert Uytterhoeven <geert+renesas(a)glider.be>
arm64: dts: renesas: r8a779a0: Add missing hypervisor virtual timer IRQ
Geert Uytterhoeven <geert+renesas(a)glider.be>
arm64: dts: renesas: r8a779h0: Drop "opp-shared" from opp-table-0
Cristian Ciocaltea <cristian.ciocaltea(a)collabora.com>
arm64: dts: rockchip: Fix mic-in-differential usage on rk3568-evb1-v10
Cristian Ciocaltea <cristian.ciocaltea(a)collabora.com>
arm64: dts: rockchip: Fix mic-in-differential usage on rk3566-roc-pc
Cristian Ciocaltea <cristian.ciocaltea(a)collabora.com>
arm64: dts: rockchip: Drop invalid mic-in-differential on rk3568-rock-3a
Jerome Brunet <jbrunet(a)baylibre.com>
arm64: dts: amlogic: setup hdmi system clock
Jerome Brunet <jbrunet(a)baylibre.com>
arm64: dts: amlogic: add power domain to hdmitx
Jerome Brunet <jbrunet(a)baylibre.com>
arm64: dts: amlogic: gx: correct hdmi clocks
AngeloGioacchino Del Regno <angelogioacchino.delregno(a)collabora.com>
soc: mediatek: mtk-mutex: Add MDP_TCC0 mod to MT8188 mutex table
Chen-Yu Tsai <wenst(a)chromium.org>
arm64: dts: mediatek: mt8183-kukui-jacuzzi: Add ports node for anx7625
Chen-Yu Tsai <wenst(a)chromium.org>
arm64: dts: mediatek: mt8183-pico6: Fix wake-on-X event node names
Hsin-Te Yuan <yuanhsinte(a)chromium.org>
arm64: dts: mediatek: mt8183-kukui: Fix the value of `dlg,jack-det-rate` mismatch
Rafał Miłecki <rafal(a)milecki.pl>
arm64: dts: mediatek: mt7622: fix "emmc" pinctrl mux
Rafał Miłecki <rafal(a)milecki.pl>
arm64: dts: mediatek: mt7981: fix code alignment for PWM clocks
Pin-yen Lin <treapking(a)chromium.org>
arm64: dts: mediatek: mt8192-asurada: Add off-on-delay-us for pp3300_mipibrdg
Chen-Yu Tsai <wenst(a)chromium.org>
arm64: dts: mediatek: mt8183-kukui: Drop bogus output-enable property
AngeloGioacchino Del Regno <angelogioacchino.delregno(a)collabora.com>
arm64: dts: medaitek: mt8395-nio-12l: Set i2c6 pins to bias-disable
AngeloGioacchino Del Regno <angelogioacchino.delregno(a)collabora.com>
arm64: dts: mediatek: mt8192: Fix GPU thermal zone name for SVS
AngeloGioacchino Del Regno <angelogioacchino.delregno(a)collabora.com>
arm64: dts: mediatek: mt8195: Fix GPU thermal zone name for SVS
Michael Walle <mwalle(a)kernel.org>
ARM: dts: imx6qdl-kontron-samx6i: fix PCIe reset polarity
Michael Walle <mwalle(a)kernel.org>
ARM: dts: imx6qdl-kontron-samx6i: fix SPI0 chip selects
Michael Walle <mwalle(a)kernel.org>
ARM: dts: imx6qdl-kontron-samx6i: fix board reset
Michael Walle <mwalle(a)kernel.org>
ARM: dts: imx6qdl-kontron-samx6i: fix PHY reset
Michael Walle <mwalle(a)kernel.org>
ARM: dts: imx6qdl-kontron-samx6i: fix phy-mode
Jerome Brunet <jbrunet(a)baylibre.com>
arm64: dts: amlogic: sm1: fix spdif compatibles
Jonas Karlman <jonas(a)kwiboo.se>
arm64: dts: rockchip: Increase VOP clk rate on RK3328
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
soc: qcom: pdr: fix parsing of domains lists
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
soc: qcom: pdr: protect locator_addr with the main mutex
Sibi Sankar <quic_sibis(a)quicinc.com>
soc: qcom: icc-bwmon: Fix refcount imbalance seen during bwmon_remove
Komal Bajaj <quic_kbajaj(a)quicinc.com>
arm64: dts: qcom: qdu1000: Add secure qfprom node
Nícolas F. R. A. Prado <nfraprado(a)collabora.com>
arm64: dts: qcom: sc7180-trogdor: Disable pwmleds node where unused
Jai Luthra <j-luthra(a)ti.com>
arm64: dts: ti: k3-am62p5-sk: Fix pinmux for McASP1 TX
Jai Luthra <j-luthra(a)ti.com>
arm64: dts: ti: k3-am625-phyboard-lyra-rdk: Drop McASP AFIFOs
Jai Luthra <j-luthra(a)ti.com>
arm64: dts: ti: k3-am62-verdin: Drop McASP AFIFOs
Jai Luthra <j-luthra(a)ti.com>
arm64: dts: ti: k3-am625-beagleplay: Drop McASP AFIFOs
Jai Luthra <j-luthra(a)ti.com>
arm64: dts: ti: k3-am62p5: Drop McASP AFIFOs
Jai Luthra <j-luthra(a)ti.com>
arm64: dts: ti: k3-am62a7: Drop McASP AFIFOs
Jai Luthra <j-luthra(a)ti.com>
arm64: dts: ti: k3-am62x: Drop McASP AFIFOs
Vaishnav Achath <vaishnav.a(a)ti.com>
arm64: dts: ti: k3-j722s: Fix main domain GPIO count
Josua Mayer <josua(a)solid-run.com>
arm64: dts: ti: k3-am642-hummingboard-t: correct rs485 rts polarity
Jayesh Choudhary <j-choudhary(a)ti.com>
arm64: dts: ti: k3-am62p-main: Fix the reg-range for main_pktdma
Jayesh Choudhary <j-choudhary(a)ti.com>
arm64: dts: ti: k3-am62a-main: Fix the reg-range for main_pktdma
Jayesh Choudhary <j-choudhary(a)ti.com>
arm64: dts: ti: k3-am62-main: Fix the reg-range for main_pktdma
Esben Haabendal <esben(a)geanix.com>
memory: fsl_ifc: Make FSL_IFC config visible and selectable
Primoz Fiser <primoz.fiser(a)norik.com>
OPP: ti: Fix ti_opp_supply_probe wrong return values
Konrad Dybcio <konrad.dybcio(a)linaro.org>
arm64: dts: qcom: sc8280xp: Throttle the GPU when overheating
Konrad Dybcio <konrad.dybcio(a)linaro.org>
arm64: dts: qcom: sc8280xp-*: Remove thermal zone polling delays
Primoz Fiser <primoz.fiser(a)norik.com>
cpufreq: ti-cpufreq: Handle deferred probe with dev_err_probe()
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: qrb4210-rb2: make L9A always-on
Marek Vasut <marex(a)denx.de>
ARM: dts: stm32: Add arm,no-tick-in-suspend to STM32MP15xx STGEN timer
Pavel Löbl <pavel(a)loebl.cz>
ARM: dts: sunxi: remove duplicated entries in makefile
Jay Buddhabhatti <jay.buddhabhatti(a)amd.com>
soc: xilinx: rename cpu_number1 to dummy_cpu_number
Sagar Cheluvegowda <quic_scheluve(a)quicinc.com>
arm64: dts: qcom: sa8775p: mark ethernet devices as DMA-coherent
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: msm8996: specify UFS core_clk frequencies
Viresh Kumar <viresh.kumar(a)linaro.org>
OPP: Fix missing cleanup on error in _opp_attach_genpd()
Javier Carrasco <javier.carrasco.cruz(a)gmail.com>
cpufreq: sun50i: fix memory leak in dt_has_supported_hw()
Jonas Karlman <jonas(a)kwiboo.se>
arm64: dts: rockchip: Update WIFi/BT related nodes on rk3308-rock-pi-s
Jonas Karlman <jonas(a)kwiboo.se>
arm64: dts: rockchip: Add mdio and ethernet-phy nodes to rk3308-rock-pi-s
Jonas Karlman <jonas(a)kwiboo.se>
arm64: dts: rockchip: Add pinctrl for UART0 to rk3308-rock-pi-s
Jonas Karlman <jonas(a)kwiboo.se>
arm64: dts: rockchip: Add sdmmc related properties on rk3308-rock-pi-s
Stephen Boyd <swboyd(a)chromium.org>
soc: qcom: rpmh-rsc: Ensure irqs aren't disabled by rpmh_rsc_send_data() callers
Chen Ni <nichen(a)iscas.ac.cn>
soc: qcom: pmic_glink: Handle the return value of pmic_glink_init
Marc Gonzalez <mgonzalez(a)freebox.fr>
arm64: dts: qcom: msm8998: enable adreno_smmu by default
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: sdm850-lenovo-yoga-c630: fix IPA firmware path
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: msm8996-xiaomi-common: drop excton from the USB PHY
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: sm8450: add power-domain to UFS PHY
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: sm8350: add power-domain to UFS PHY
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: sm8250: add power-domain to UFS PHY
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: sm6350: add power-domain to UFS PHY
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: sm6115: add power-domain to UFS PHY
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: sdm845: add power-domain to UFS PHY
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: sc8180x: add power-domain to UFS PHY
Dmitry Baryshkov <dmitry.baryshkov(a)linaro.org>
arm64: dts: qcom: sc7180: drop extra UFS PHY compat
Rayyan Ansari <rayyan(a)ansari.sh>
ARM: dts: qcom: msm8226-microsoft-common: Enable smbb explicitly
Viken Dadhaniya <quic_vdadhani(a)quicinc.com>
arm64: dts: qcom: sc7280: Remove CTS/RTS configuration
Bjorn Andersson <quic_bjorande(a)quicinc.com>
arm64: dts: qcom: sc8180x: Correct PCIe slave ports
Konrad Dybcio <konrad.dybcio(a)linaro.org>
soc: qcom: socinfo: Update X1E PMICs
Guenter Roeck <linux(a)roeck-us.net>
hwmon: (max6697) Fix swapped temp{1,8} critical alarms
Guenter Roeck <linux(a)roeck-us.net>
hwmon: (max6697) Fix underflow when writing limit attributes
Nirmoy Das <nirmoy.das(a)intel.com>
drm/xe/display/xe_hdcp_gsc: Free arbiter on driver removal
Uwe Kleine-König <u.kleine-koenig(a)baylibre.com>
pwm: atmel-tcb: Fix race condition and convert to guards
Yao Zi <ziyao(a)disroot.org>
drm/meson: fix canvas release in bind function
Gaosheng Cui <cuigaosheng1(a)huawei.com>
nvmet-auth: fix nvmet_auth hash error handling
Jinjie Ruan <ruanjinjie(a)huawei.com>
arm64: smp: Fix missing IPI statistics
Adam Ford <aford173(a)gmail.com>
drm/bridge: adv7511: Fix Intermittent EDID failures
Uwe Kleine-König <u.kleine-koenig(a)baylibre.com>
pwm: stm32: Always do lazy disabling
Dan Carpenter <dan.carpenter(a)linaro.org>
hwmon: (ltc2991) re-order conditions to fix off by one bug
Benjamin Marzinski <bmarzins(a)redhat.com>
md/raid5: recheck if reshape has finished with device_lock held
Yu Kuai <yukuai3(a)huawei.com>
md: Don't wait for MD_RECOVERY_NEEDED for HOT_REMOVE_DISK ioctl
Rob Herring (Arm) <robh(a)kernel.org>
perf: arm_pmuv3: Avoid assigning fixed cycle counter with threshold
Christoph Hellwig <hch(a)lst.de>
xen-blkfront: fix sector_size propagation to the block layer
Bart Van Assche <bvanassche(a)acm.org>
block/mq-deadline: Fix the tag reservation code
Bart Van Assche <bvanassche(a)acm.org>
block: Call .limit_depth() after .hctx has been set
Wayne Tung <chineweff(a)gmail.com>
hwmon: (adt7475) Fix default duty on fan is disabled
Chen Ridong <chenridong(a)huawei.com>
cgroup/cpuset: Prevent UAF in proc_cpuset_show()
Josh Poimboeuf <jpoimboe(a)kernel.org>
x86/syscall: Mark exit[_group] syscall handlers __noreturn
Ilpo Järvinen <ilpo.jarvinen(a)linux.intel.com>
x86/platform/iosf_mbi: Convert PCIBIOS_* return codes to errnos
Ilpo Järvinen <ilpo.jarvinen(a)linux.intel.com>
x86/pci/xen: Fix PCIBIOS_* return code handling
Ilpo Järvinen <ilpo.jarvinen(a)linux.intel.com>
x86/pci/intel_mid_pci: Fix PCIBIOS_* return code handling
Ilpo Järvinen <ilpo.jarvinen(a)linux.intel.com>
x86/of: Return consistent error type from x86_of_pci_irq_enable()
Chao Yu <chao(a)kernel.org>
hfsplus: fix to avoid false alarm of circular locking
Masahiro Yamada <masahiroy(a)kernel.org>
x86/kconfig: Add as-instr64 macro to properly evaluate AS_WRUSS
Waiman Long <longman(a)redhat.com>
cgroup/cpuset: Fix remote root partition creation problem
Waiman Long <longman(a)redhat.com>
cgroup/cpuset: Optimize isolated partition only generate_sched_domains() calls
Gabriel Krisman Bertazi <krisman(a)suse.de>
io_uring: Fix probe of disabled operations
Damien Le Moal <dlemoal(a)kernel.org>
dm: Call dm_revalidate_zones() after setting the queue limits
Christoph Hellwig <hch(a)lst.de>
block: initialize integrity buffer to zero before writing it to media
Christoph Hellwig <hch(a)lst.de>
ubd: untagle discard vs write zeroes not support handling
Christoph Hellwig <hch(a)lst.de>
ubd: refactor the interrupt handler
Tzung-Bi Shih <tzungbi(a)kernel.org>
platform/chrome: cros_ec_debugfs: fix wrong EC message version
Christoph Hellwig <hch(a)lst.de>
md/raid1: don't free conf on raid0_run failure
Christoph Hellwig <hch(a)lst.de>
md/raid0: don't free conf on raid0_run failure
Li Nan <linan122(a)huawei.com>
md: fix deadlock between mddev_suspend and flush bio
Frederic Weisbecker <frederic(a)kernel.org>
rcu/tasks: Fix stale task snaphot for Tasks Trace
Arnd Bergmann <arnd(a)arndb.de>
EDAC, i10nm: make skx_common.o a separate module
Chen Ni <nichen(a)iscas.ac.cn>
spi: atmel-quadspi: Add missing check for clk_prepare
Prajna Rajendra Kumar <prajna.rajendrakumar(a)microchip.com>
spi: spi-microchip-core: Fix the number of chip selects supported
-------------
Diffstat:
Documentation/admin-guide/kernel-parameters.txt | 4 +-
Documentation/arch/powerpc/kvm-nested.rst | 4 +-
.../phy/qcom,sc8280xp-qmp-usb3-uni-phy.yaml | 2 +-
.../devicetree/bindings/thermal/thermal-zones.yaml | 5 +-
Documentation/networking/xsk-tx-metadata.rst | 16 +-
Documentation/virt/kvm/api.rst | 12 +
Makefile | 4 +-
arch/arm/boot/dts/allwinner/Makefile | 62 --
.../arm/boot/dts/nxp/imx/imx6q-kontron-samx6i.dtsi | 23 -
.../boot/dts/nxp/imx/imx6qdl-kontron-samx6i.dtsi | 14 +-
.../dts/qcom/qcom-msm8226-microsoft-common.dtsi | 4 +
arch/arm/boot/dts/st/stm32mp151.dtsi | 1 +
arch/arm/mach-pxa/spitz.c | 30 +-
arch/arm/mm/fault.c | 4 +-
arch/arm64/boot/dts/amlogic/meson-g12-common.dtsi | 5 +
arch/arm64/boot/dts/amlogic/meson-g12.dtsi | 4 +
arch/arm64/boot/dts/amlogic/meson-gxbb.dtsi | 10 +-
arch/arm64/boot/dts/amlogic/meson-gxl.dtsi | 10 +-
arch/arm64/boot/dts/amlogic/meson-sm1.dtsi | 8 +-
arch/arm64/boot/dts/freescale/imx8mp.dtsi | 89 +--
.../boot/dts/mediatek/mt7622-bananapi-bpi-r64.dts | 4 +-
arch/arm64/boot/dts/mediatek/mt7622-rfb1.dts | 4 +-
arch/arm64/boot/dts/mediatek/mt7981b.dtsi | 8 +-
.../dts/mediatek/mt8183-kukui-audio-da7219.dtsi | 2 +-
.../dts/mediatek/mt8183-kukui-jacuzzi-pico6.dts | 8 +-
.../boot/dts/mediatek/mt8183-kukui-jacuzzi.dtsi | 25 +-
arch/arm64/boot/dts/mediatek/mt8183-kukui.dtsi | 4 +-
arch/arm64/boot/dts/mediatek/mt8192-asurada.dtsi | 1 +
arch/arm64/boot/dts/mediatek/mt8192.dtsi | 2 +-
arch/arm64/boot/dts/mediatek/mt8195.dtsi | 2 +-
.../boot/dts/mediatek/mt8395-radxa-nio-12l.dts | 2 +-
.../arm64/boot/dts/qcom/msm8996-xiaomi-common.dtsi | 1 -
arch/arm64/boot/dts/qcom/msm8996.dtsi | 2 +-
arch/arm64/boot/dts/qcom/msm8998.dtsi | 1 -
arch/arm64/boot/dts/qcom/qcm6490-fairphone-fp5.dts | 1 -
arch/arm64/boot/dts/qcom/qcm6490-idp.dts | 1 -
arch/arm64/boot/dts/qcom/qcs6490-rb3gen2.dts | 1 -
arch/arm64/boot/dts/qcom/qdu1000.dtsi | 15 +
arch/arm64/boot/dts/qcom/qrb4210-rb2.dts | 4 +-
arch/arm64/boot/dts/qcom/sa8775p.dtsi | 2 +
.../boot/dts/qcom/sc7180-trogdor-lazor-r1-kb.dts | 2 +-
.../boot/dts/qcom/sc7180-trogdor-lazor-r1-lte.dts | 2 +-
.../boot/dts/qcom/sc7180-trogdor-lazor-r10-kb.dts | 2 +-
.../boot/dts/qcom/sc7180-trogdor-lazor-r10-lte.dts | 2 +-
.../boot/dts/qcom/sc7180-trogdor-lazor-r3-kb.dts | 2 +-
.../boot/dts/qcom/sc7180-trogdor-lazor-r3-lte.dts | 2 +-
.../boot/dts/qcom/sc7180-trogdor-lazor-r9-kb.dts | 2 +-
.../boot/dts/qcom/sc7180-trogdor-lazor-r9-lte.dts | 2 +-
arch/arm64/boot/dts/qcom/sc7180-trogdor.dtsi | 5 +-
arch/arm64/boot/dts/qcom/sc7180.dtsi | 3 +-
arch/arm64/boot/dts/qcom/sc7280-idp.dtsi | 1 -
arch/arm64/boot/dts/qcom/sc7280-qcard.dtsi | 1 -
arch/arm64/boot/dts/qcom/sc7280.dtsi | 14 +-
arch/arm64/boot/dts/qcom/sc8180x.dtsi | 8 +-
.../dts/qcom/sc8280xp-lenovo-thinkpad-x13s.dts | 2 +-
arch/arm64/boot/dts/qcom/sc8280xp-pmics.dtsi | 4 +-
arch/arm64/boot/dts/qcom/sc8280xp.dtsi | 28 +-
arch/arm64/boot/dts/qcom/sdm845.dtsi | 2 +
.../boot/dts/qcom/sdm850-lenovo-yoga-c630.dts | 1 +
arch/arm64/boot/dts/qcom/sm6115.dtsi | 2 +
arch/arm64/boot/dts/qcom/sm6350.dtsi | 4 +
arch/arm64/boot/dts/qcom/sm8250.dtsi | 2 +
arch/arm64/boot/dts/qcom/sm8350.dtsi | 2 +
arch/arm64/boot/dts/qcom/sm8450.dtsi | 2 +
arch/arm64/boot/dts/qcom/x1e80100-crd.dts | 6 +-
arch/arm64/boot/dts/qcom/x1e80100-qcp.dts | 6 +-
arch/arm64/boot/dts/renesas/r8a779a0.dtsi | 5 +-
arch/arm64/boot/dts/renesas/r8a779f0.dtsi | 5 +-
arch/arm64/boot/dts/renesas/r8a779g0.dtsi | 5 +-
arch/arm64/boot/dts/renesas/r8a779h0.dtsi | 1 -
arch/arm64/boot/dts/renesas/r9a07g043u.dtsi | 5 +-
arch/arm64/boot/dts/renesas/r9a07g044.dtsi | 5 +-
arch/arm64/boot/dts/renesas/r9a07g054.dtsi | 5 +-
arch/arm64/boot/dts/renesas/r9a08g045.dtsi | 5 +-
arch/arm64/boot/dts/rockchip/rk3308-rock-pi-s.dts | 71 +-
arch/arm64/boot/dts/rockchip/rk3328.dtsi | 4 +-
arch/arm64/boot/dts/rockchip/rk3566-roc-pc.dts | 2 +-
arch/arm64/boot/dts/rockchip/rk3568-evb1-v10.dts | 2 +-
.../boot/dts/rockchip/rk3568-fastrhino-r66s.dts | 4 +
.../boot/dts/rockchip/rk3568-fastrhino-r66s.dtsi | 48 +-
.../boot/dts/rockchip/rk3568-fastrhino-r68s.dts | 16 +-
arch/arm64/boot/dts/rockchip/rk3568-rock-3a.dts | 4 -
arch/arm64/boot/dts/rockchip/rk356x.dtsi | 1 +
arch/arm64/boot/dts/ti/k3-am62-main.dtsi | 4 +-
arch/arm64/boot/dts/ti/k3-am62-verdin.dtsi | 4 -
arch/arm64/boot/dts/ti/k3-am625-beagleplay.dts | 2 -
.../boot/dts/ti/k3-am625-phyboard-lyra-rdk.dts | 2 -
arch/arm64/boot/dts/ti/k3-am62a-main.dtsi | 4 +-
arch/arm64/boot/dts/ti/k3-am62a7-sk.dts | 2 -
arch/arm64/boot/dts/ti/k3-am62p-main.dtsi | 4 +-
arch/arm64/boot/dts/ti/k3-am62p5-sk.dts | 4 +-
arch/arm64/boot/dts/ti/k3-am62x-sk-common.dtsi | 2 -
arch/arm64/boot/dts/ti/k3-am642-hummingboard-t.dts | 1 -
arch/arm64/boot/dts/ti/k3-j722s.dtsi | 8 +
arch/arm64/include/asm/pgtable.h | 22 +
arch/arm64/kernel/smp.c | 6 +-
arch/arm64/net/bpf_jit_comp.c | 4 +-
arch/loongarch/kernel/hw_breakpoint.c | 2 +-
arch/loongarch/kernel/ptrace.c | 3 +
arch/m68k/amiga/config.c | 9 +
arch/m68k/atari/ataints.c | 6 +-
arch/m68k/include/asm/cmpxchg.h | 2 +-
arch/mips/Makefile | 2 +-
arch/mips/boot/dts/loongson/loongson64-2k1000.dtsi | 21 +-
arch/mips/include/asm/mach-loongson64/boot_param.h | 2 +
arch/mips/include/asm/mips-cm.h | 4 +
arch/mips/kernel/smp-cps.c | 5 +-
arch/mips/loongson64/env.c | 8 +
arch/mips/loongson64/reset.c | 38 +-
arch/mips/loongson64/smp.c | 23 +-
arch/mips/pci/pcie-octeon.c | 0
arch/mips/sgi-ip30/ip30-console.c | 1 +
arch/parisc/Kconfig | 1 +
arch/powerpc/include/asm/guest-state-buffer.h | 3 +-
arch/powerpc/include/asm/kvm_book3s.h | 1 +
arch/powerpc/kernel/prom.c | 12 +-
arch/powerpc/kexec/core_64.c | 55 +-
arch/powerpc/kvm/book3s_hv.c | 9 +-
arch/powerpc/kvm/book3s_hv_nestedv2.c | 7 +
arch/powerpc/kvm/powerpc.c | 4 +-
arch/powerpc/kvm/test-guest-state-buffer.c | 2 +-
arch/powerpc/mm/nohash/8xx.c | 3 +-
arch/powerpc/xmon/ppc-dis.c | 33 +-
arch/riscv/kernel/head.S | 19 +-
arch/riscv/kernel/smpboot.c | 14 +-
arch/riscv/net/bpf_jit_comp64.c | 18 +-
arch/s390/kernel/perf_cpum_cf.c | 14 +-
arch/s390/kernel/setup.c | 2 +-
arch/s390/kernel/uv.c | 8 +
arch/s390/kvm/kvm-s390.c | 3 +
arch/s390/pci/pci_irq.c | 110 ++--
arch/sparc/include/asm/oplib_64.h | 1 +
arch/sparc/prom/init_64.c | 3 -
arch/sparc/prom/p1275.c | 2 +-
arch/um/drivers/ubd_kern.c | 50 +-
arch/um/kernel/time.c | 4 +-
arch/um/os-Linux/signal.c | 118 +++-
arch/x86/Kconfig.assembler | 2 +-
arch/x86/Makefile.um | 1 +
arch/x86/entry/syscall_32.c | 10 +-
arch/x86/entry/syscall_64.c | 9 +-
arch/x86/entry/syscall_x32.c | 7 +-
arch/x86/entry/syscalls/syscall_32.tbl | 6 +-
arch/x86/entry/syscalls/syscall_64.tbl | 6 +-
arch/x86/events/amd/uncore.c | 28 +-
arch/x86/events/core.c | 3 +
arch/x86/events/intel/cstate.c | 7 +-
arch/x86/events/intel/ds.c | 8 +-
arch/x86/events/intel/pt.c | 4 +-
arch/x86/events/intel/pt.h | 4 +-
arch/x86/events/intel/uncore_snbep.c | 6 +-
arch/x86/include/asm/kvm-x86-ops.h | 1 -
arch/x86/include/asm/kvm_host.h | 3 +-
arch/x86/include/asm/shstk.h | 2 +
arch/x86/kernel/devicetree.c | 2 +-
arch/x86/kernel/shstk.c | 11 +
arch/x86/kernel/uprobes.c | 7 +-
arch/x86/kvm/vmx/main.c | 1 -
arch/x86/kvm/vmx/nested.c | 47 +-
arch/x86/kvm/vmx/posted_intr.h | 10 +
arch/x86/kvm/vmx/vmx.c | 31 +-
arch/x86/kvm/vmx/vmx.h | 1 +
arch/x86/kvm/vmx/x86_ops.h | 1 -
arch/x86/kvm/x86.c | 14 +-
arch/x86/pci/intel_mid_pci.c | 4 +-
arch/x86/pci/xen.c | 4 +-
arch/x86/platform/intel/iosf_mbi.c | 4 +-
arch/x86/um/sys_call_table_32.c | 10 +-
arch/x86/um/sys_call_table_64.c | 11 +-
arch/x86/virt/svm/sev.c | 44 +-
arch/x86/xen/p2m.c | 4 +-
block/bio-integrity.c | 11 +-
block/blk-mq.c | 32 +-
block/genhd.c | 2 +-
block/mq-deadline.c | 20 +-
drivers/android/binder.c | 4 +-
drivers/ata/libata-scsi.c | 176 ++---
drivers/auxdisplay/ht16k33.c | 1 +
drivers/base/devres.c | 11 +-
drivers/block/null_blk/main.c | 2 +-
drivers/block/rbd.c | 35 +-
drivers/block/ublk_drv.c | 5 +-
drivers/block/xen-blkfront.c | 16 +-
drivers/bluetooth/btintel.c | 119 +---
drivers/bluetooth/btintel_pcie.c | 6 +
drivers/bluetooth/btnxpuart.c | 52 +-
drivers/bluetooth/btusb.c | 4 +
drivers/bluetooth/hci_bcm4377.c | 2 +-
drivers/bus/mhi/ep/main.c | 14 +-
drivers/char/hw_random/amd-rng.c | 4 +-
drivers/char/hw_random/core.c | 4 +-
drivers/char/ipmi/ssif_bmc.c | 6 +-
drivers/char/tpm/eventlog/common.c | 2 +
drivers/char/tpm/tpm_tis_spi_main.c | 1 +
drivers/clk/clk-en7523.c | 9 +-
drivers/clk/davinci/da8xx-cfgchip.c | 4 +-
drivers/clk/meson/s4-peripherals.c | 2 +-
drivers/clk/meson/s4-pll.c | 5 +
drivers/clk/qcom/camcc-sc7280.c | 5 +
drivers/clk/qcom/clk-rcg2.c | 32 +
drivers/clk/qcom/gcc-sa8775p.c | 40 ++
drivers/clk/qcom/gcc-sc7280.c | 3 +
drivers/clk/qcom/gcc-x1e80100.c | 46 +-
drivers/clk/qcom/gpucc-sa8775p.c | 41 +-
drivers/clk/qcom/gpucc-sm8350.c | 5 +-
drivers/clk/qcom/kpss-xcc.c | 4 +-
drivers/clk/samsung/clk-exynos4.c | 13 +-
drivers/cpufreq/amd-pstate-ut.c | 12 +-
drivers/cpufreq/amd-pstate.c | 43 +-
drivers/cpufreq/qcom-cpufreq-nvmem.c | 13 +-
drivers/cpufreq/sun50i-cpufreq-nvmem.c | 4 +-
drivers/cpufreq/ti-cpufreq.c | 2 +-
drivers/crypto/atmel-sha204a.c | 2 +-
drivers/crypto/ccp/sev-dev.c | 8 +-
drivers/crypto/intel/qat/qat_common/adf_cfg.c | 6 +-
drivers/crypto/mxs-dcp.c | 3 +-
drivers/crypto/tegra/tegra-se-main.c | 1 -
drivers/dma/fsl-edma-common.c | 3 +
drivers/dma/fsl-edma-common.h | 1 +
drivers/dma/fsl-edma-main.c | 2 +-
drivers/dma/ti/k3-udma.c | 4 +-
drivers/edac/Makefile | 10 +-
drivers/edac/skx_common.c | 21 +-
drivers/edac/skx_common.h | 4 +-
drivers/firmware/efi/libstub/screen_info.c | 2 +
drivers/firmware/efi/libstub/x86-stub.c | 25 +-
drivers/firmware/turris-mox-rwtm.c | 23 +-
drivers/gpu/drm/Kconfig | 3 +-
drivers/gpu/drm/amd/amdgpu/amdgpu_device.c | 2 +-
drivers/gpu/drm/amd/amdgpu/amdgpu_gfx.c | 5 +-
drivers/gpu/drm/amd/amdgpu/amdgpu_gmc.c | 1 -
drivers/gpu/drm/amd/amdgpu/amdgpu_vm.c | 9 +-
drivers/gpu/drm/amd/amdgpu/gmc_v9_0.c | 2 +-
drivers/gpu/drm/amd/amdgpu/sdma_v5_2.c | 12 +
drivers/gpu/drm/amd/amdgpu/smu_v13_0_10.c | 2 +-
drivers/gpu/drm/amd/amdgpu/vcn_v4_0.c | 6 +
drivers/gpu/drm/amd/amdgpu/vcn_v4_0_5.c | 6 +
drivers/gpu/drm/amd/amdgpu/vcn_v5_0_0.c | 6 +
drivers/gpu/drm/amd/amdkfd/kfd_mqd_manager_v9.c | 2 +-
drivers/gpu/drm/amd/display/dc/core/dc_surface.c | 3 +-
drivers/gpu/drm/amd/display/dc/dc.h | 1 +
.../drm/amd/display/dc/dml2/dml2_mall_phantom.c | 2 +
.../amd/display/dc/dml2/dml2_translation_helper.c | 56 +-
.../gpu/drm/amd/display/dc/optc/dcn10/dcn10_optc.c | 15 +-
.../gpu/drm/amd/display/dc/optc/dcn20/dcn20_optc.c | 10 +
.../amd/display/dc/resource/dcn32/dcn32_resource.c | 12 +-
.../display/dc/resource/dcn321/dcn321_resource.c | 12 +-
.../gpu/drm/amd/display/include/grph_object_id.h | 4 +-
drivers/gpu/drm/amd/pm/swsmu/smu13/smu_v13_0.c | 4 +-
drivers/gpu/drm/arm/display/komeda/komeda_crtc.c | 43 +-
drivers/gpu/drm/bridge/adv7511/adv7511.h | 2 +-
drivers/gpu/drm/bridge/adv7511/adv7511_cec.c | 13 +-
drivers/gpu/drm/bridge/adv7511/adv7511_drv.c | 22 +-
drivers/gpu/drm/bridge/ite-it6505.c | 81 ++-
drivers/gpu/drm/bridge/samsung-dsim.c | 4 +-
drivers/gpu/drm/display/drm_dp_mst_topology.c | 4 +-
drivers/gpu/drm/drm_fbdev_dma.c | 3 +-
drivers/gpu/drm/drm_panic.c | 70 +-
drivers/gpu/drm/etnaviv/etnaviv_gem.c | 6 +-
drivers/gpu/drm/etnaviv/etnaviv_sched.c | 9 +-
drivers/gpu/drm/gma500/cdv_intel_lvds.c | 3 +
drivers/gpu/drm/gma500/psb_intel_lvds.c | 3 +
.../gpu/drm/i915/display/intel_crtc_state_dump.c | 7 +-
drivers/gpu/drm/i915/display/intel_display.c | 6 +-
drivers/gpu/drm/i915/display/intel_display_types.h | 2 +-
drivers/gpu/drm/i915/display/intel_dp.c | 4 +-
.../gpu/drm/i915/display/intel_dp_link_training.c | 55 +-
drivers/gpu/drm/i915/display/intel_fbc.c | 2 +-
drivers/gpu/drm/i915/display/intel_psr.c | 36 +-
.../gpu/drm/i915/gt/intel_execlists_submission.c | 6 +-
drivers/gpu/drm/mediatek/mtk_ddp_comp.c | 107 +--
drivers/gpu/drm/mediatek/mtk_ddp_comp.h | 8 +-
drivers/gpu/drm/mediatek/mtk_disp_ovl.c | 41 +-
drivers/gpu/drm/mediatek/mtk_disp_ovl_adaptor.c | 2 +-
drivers/gpu/drm/mediatek/mtk_dp.c | 10 +-
drivers/gpu/drm/mediatek/mtk_dpi.c | 5 +-
drivers/gpu/drm/mediatek/mtk_drm_drv.c | 24 +
drivers/gpu/drm/mediatek/mtk_drm_drv.h | 4 +
drivers/gpu/drm/mediatek/mtk_dsi.c | 5 +-
drivers/gpu/drm/mediatek/mtk_ethdr.c | 21 +-
drivers/gpu/drm/mediatek/mtk_plane.c | 4 +-
drivers/gpu/drm/meson/meson_drv.c | 37 +-
drivers/gpu/drm/msm/adreno/a6xx_gpu.c | 2 +-
drivers/gpu/drm/msm/adreno/a6xx_gpu_state.c | 13 +-
drivers/gpu/drm/msm/disp/dpu1/dpu_encoder.c | 7 +-
drivers/gpu/drm/msm/disp/dpu1/dpu_encoder_phys.h | 5 +
.../gpu/drm/msm/disp/dpu1/dpu_encoder_phys_cmd.c | 32 +-
.../gpu/drm/msm/disp/dpu1/dpu_encoder_phys_vid.c | 13 +-
.../gpu/drm/msm/disp/dpu1/dpu_encoder_phys_wb.c | 14 +-
drivers/gpu/drm/msm/disp/dpu1/dpu_hw_catalog.c | 6 -
drivers/gpu/drm/msm/disp/dpu1/dpu_hw_ctl.h | 3 +-
drivers/gpu/drm/msm/dp/dp_aux.c | 5 +-
drivers/gpu/drm/msm/dsi/dsi_host.c | 6 +-
drivers/gpu/drm/panel/panel-boe-tv101wum-nl6.c | 8 +-
drivers/gpu/drm/panel/panel-himax-hx8394.c | 3 +-
drivers/gpu/drm/panel/panel-ilitek-ili9882t.c | 8 +-
drivers/gpu/drm/panel/panel-lg-sw43408.c | 33 +-
drivers/gpu/drm/panfrost/panfrost_drv.c | 1 +
drivers/gpu/drm/panthor/panthor_sched.c | 1 +
drivers/gpu/drm/qxl/qxl_display.c | 17 +-
drivers/gpu/drm/qxl/qxl_object.c | 13 +-
drivers/gpu/drm/qxl/qxl_object.h | 4 +-
drivers/gpu/drm/rockchip/rockchip_drm_vop2.c | 2 +-
drivers/gpu/drm/ttm/tests/ttm_bo_test.c | 48 +-
drivers/gpu/drm/ttm/tests/ttm_kunit_helpers.c | 7 +-
drivers/gpu/drm/ttm/tests/ttm_kunit_helpers.h | 3 +-
drivers/gpu/drm/ttm/tests/ttm_pool_test.c | 4 +-
drivers/gpu/drm/ttm/tests/ttm_resource_test.c | 2 +-
drivers/gpu/drm/ttm/tests/ttm_tt_test.c | 20 +-
drivers/gpu/drm/udl/udl_modeset.c | 3 +-
drivers/gpu/drm/xe/display/xe_hdcp_gsc.c | 12 +-
drivers/gpu/drm/xe/xe_bo.c | 47 +-
drivers/gpu/drm/xe/xe_bo_types.h | 3 +-
drivers/gpu/drm/xe/xe_exec.c | 14 +-
drivers/gpu/drm/xe/xe_gt_sriov_pf_config.c | 1 +
drivers/gpu/drm/xlnx/zynqmp_dpsub.c | 1 +
drivers/gpu/drm/xlnx/zynqmp_kms.c | 12 +-
drivers/hwmon/adt7475.c | 2 +-
drivers/hwmon/ltc2991.c | 4 +-
drivers/hwmon/max6697.c | 5 +-
drivers/hwtracing/coresight/coresight-platform.c | 4 +-
drivers/i3c/master/mipi-i3c-hci/core.c | 8 +
drivers/iio/adc/ad9467.c | 65 +-
drivers/iio/adc/adi-axi-adc.c | 2 +
drivers/iio/frequency/adrf6780.c | 1 -
drivers/iio/industrialio-gts-helper.c | 7 +-
drivers/infiniband/core/cache.c | 14 +-
drivers/infiniband/core/device.c | 14 +-
drivers/infiniband/core/iwcm.c | 11 +-
drivers/infiniband/hw/bnxt_re/ib_verbs.c | 8 +-
drivers/infiniband/hw/bnxt_re/qplib_fp.h | 6 +-
drivers/infiniband/hw/hns/hns_roce_device.h | 7 +
drivers/infiniband/hw/hns/hns_roce_hw_v2.c | 164 +++--
drivers/infiniband/hw/hns/hns_roce_hw_v2.h | 6 +
drivers/infiniband/hw/hns/hns_roce_mr.c | 5 +
drivers/infiniband/hw/hns/hns_roce_qp.c | 4 +-
drivers/infiniband/hw/hns/hns_roce_srq.c | 2 +-
drivers/infiniband/hw/mana/device.c | 16 +-
drivers/infiniband/hw/mlx4/alias_GUID.c | 2 +-
drivers/infiniband/hw/mlx4/mad.c | 2 +-
drivers/infiniband/hw/mlx5/mlx5_ib.h | 13 +
drivers/infiniband/hw/mlx5/odp.c | 6 +-
drivers/infiniband/sw/rxe/rxe_req.c | 7 +-
drivers/input/keyboard/qt1050.c | 7 +-
drivers/input/mouse/elan_i2c_core.c | 2 +
drivers/interconnect/qcom/qcm2290.c | 2 +-
drivers/iommu/arm/arm-smmu-v3/arm-smmu-v3.c | 2 +-
drivers/iommu/arm/arm-smmu/arm-smmu-qcom-debug.c | 17 +-
drivers/iommu/arm/arm-smmu/arm-smmu-qcom.c | 39 ++
drivers/iommu/arm/arm-smmu/arm-smmu-qcom.h | 2 +
drivers/iommu/intel/cache.c | 3 +-
drivers/iommu/intel/iommu.c | 2 +-
drivers/iommu/iommufd/iova_bitmap.c | 5 +-
drivers/iommu/iommufd/selftest.c | 2 +-
drivers/iommu/sprd-iommu.c | 2 +-
drivers/irqchip/irq-imx-irqsteer.c | 24 +-
drivers/isdn/hardware/mISDN/hfcmulti.c | 7 +-
drivers/leds/flash/leds-mt6360.c | 5 +-
drivers/leds/flash/leds-qcom-flash.c | 10 +-
drivers/leds/led-class.c | 1 -
drivers/leds/led-triggers.c | 8 +-
drivers/leds/leds-ss4200.c | 7 +-
drivers/leds/rgb/leds-qcom-lpg.c | 8 +-
drivers/leds/trigger/ledtrig-timer.c | 5 -
drivers/macintosh/therm_windtunnel.c | 2 +-
drivers/mailbox/imx-mailbox.c | 10 +-
drivers/mailbox/mtk-cmdq-mailbox.c | 12 +-
drivers/mailbox/omap-mailbox.c | 3 +-
drivers/md/dm-raid.c | 7 +-
drivers/md/dm-table.c | 15 +-
drivers/md/dm-verity-target.c | 16 +-
drivers/md/dm-zone.c | 25 +-
drivers/md/dm.h | 1 +
drivers/md/md-bitmap.c | 6 +-
drivers/md/md-cluster.c | 22 +-
drivers/md/md.c | 32 +-
drivers/md/raid0.c | 21 +-
drivers/md/raid1.c | 15 +-
drivers/md/raid5.c | 76 ++-
drivers/media/i2c/Kconfig | 1 +
drivers/media/i2c/alvium-csi2.c | 6 +-
drivers/media/i2c/hi846.c | 2 +-
drivers/media/i2c/imx219.c | 2 +-
drivers/media/i2c/imx412.c | 9 +-
drivers/media/pci/intel/ivsc/mei_csi.c | 14 +-
drivers/media/pci/ivtv/ivtv-udma.c | 8 +
drivers/media/pci/ivtv/ivtv-yuv.c | 6 +
drivers/media/pci/ivtv/ivtvfb.c | 6 +-
drivers/media/pci/saa7134/saa7134-dvb.c | 8 +-
.../mediatek/vcodec/decoder/vdec/vdec_vp8_if.c | 2 +-
.../platform/mediatek/vcodec/decoder/vdec_vpu_if.c | 6 +
drivers/media/platform/nxp/imx-jpeg/mxc-jpeg.c | 3 +
drivers/media/platform/nxp/imx-pxp.c | 3 +
drivers/media/platform/qcom/venus/vdec.c | 3 +-
drivers/media/platform/renesas/rcar-csi2.c | 5 +-
drivers/media/platform/renesas/rcar-vin/rcar-dma.c | 16 +-
drivers/media/platform/renesas/vsp1/vsp1_histo.c | 20 +-
drivers/media/platform/renesas/vsp1/vsp1_pipe.h | 2 +-
drivers/media/platform/renesas/vsp1/vsp1_rpf.c | 8 +-
.../platform/st/sti/c8sectpfe/c8sectpfe-debugfs.h | 4 +-
.../platform/st/stm32/stm32-dcmipp/dcmipp-core.c | 4 +-
drivers/media/rc/imon.c | 5 +-
drivers/media/rc/lirc_dev.c | 4 +-
drivers/media/usb/dvb-usb/dvb-usb-init.c | 35 +-
drivers/media/usb/uvc/uvc_ctrl.c | 9 +-
drivers/media/usb/uvc/uvc_driver.c | 12 +-
drivers/media/usb/uvc/uvc_video.c | 21 +-
drivers/media/usb/uvc/uvcvideo.h | 1 +
drivers/media/v4l2-core/v4l2-async.c | 3 +
drivers/memory/Kconfig | 2 +-
drivers/mfd/Makefile | 6 +-
drivers/mfd/omap-usb-tll.c | 3 +-
drivers/mfd/rsmu_core.c | 2 +
drivers/misc/eeprom/ee1004.c | 6 +-
drivers/mtd/nand/raw/Kconfig | 3 +-
drivers/mtd/spi-nor/winbond.c | 2 +
drivers/mtd/tests/Makefile | 34 +-
drivers/mtd/tests/mtd_test.c | 9 +
drivers/mtd/ubi/eba.c | 3 +-
drivers/net/bonding/bond_main.c | 7 +-
drivers/net/dsa/b53/b53_common.c | 3 +
drivers/net/dsa/microchip/ksz_common.c | 7 +
drivers/net/dsa/mv88e6xxx/chip.c | 3 +-
drivers/net/ethernet/brocade/bna/bna_types.h | 2 +-
drivers/net/ethernet/brocade/bna/bnad.c | 11 +-
drivers/net/ethernet/cortina/gemini.c | 23 +-
drivers/net/ethernet/freescale/fec_main.c | 6 +
drivers/net/ethernet/google/gve/gve_tx.c | 5 +-
drivers/net/ethernet/google/gve/gve_tx_dqo.c | 22 +-
drivers/net/ethernet/hisilicon/hns3/Makefile | 11 +-
.../hisilicon/hns3/hns3_common/hclge_comm_cmd.c | 11 +
.../hisilicon/hns3/hns3_common/hclge_comm_rss.c | 14 +
.../hns3/hns3_common/hclge_comm_tqp_stats.c | 5 +
drivers/net/ethernet/intel/ice/ice_ethtool_fdir.c | 2 +-
drivers/net/ethernet/intel/ice/ice_fdir.h | 3 +
drivers/net/ethernet/intel/ice/ice_switch.c | 8 +-
drivers/net/ethernet/intel/ice/ice_virtchnl_fdir.c | 16 +
drivers/net/ethernet/intel/ice/ice_virtchnl_fdir.h | 1 +
drivers/net/ethernet/mediatek/mtk_eth_soc.c | 3 +-
.../ethernet/mellanox/mlxsw/spectrum_acl_atcam.c | 18 +-
.../mellanox/mlxsw/spectrum_acl_bloom_filter.c | 2 +-
.../net/ethernet/mellanox/mlxsw/spectrum_acl_erp.c | 13 -
.../ethernet/mellanox/mlxsw/spectrum_acl_tcam.h | 9 +-
drivers/net/ethernet/microsoft/mana/mana_en.c | 19 +
drivers/net/ethernet/stmicro/stmmac/dwmac4_core.c | 2 +-
.../net/ethernet/stmicro/stmmac/dwxgmac2_core.c | 2 +-
drivers/net/ethernet/stmicro/stmmac/hwif.h | 2 +-
drivers/net/ethernet/stmicro/stmmac/stmmac_main.c | 4 +-
drivers/net/netconsole.c | 2 +-
drivers/net/pse-pd/pse_core.c | 4 +-
drivers/net/virtio_net.c | 85 ++-
drivers/net/wireless/ath/ath11k/ce.h | 6 +-
drivers/net/wireless/ath/ath11k/core.c | 29 +-
drivers/net/wireless/ath/ath11k/dp_rx.c | 3 +-
drivers/net/wireless/ath/ath11k/dp_rx.h | 3 +
drivers/net/wireless/ath/ath11k/mac.c | 28 +-
drivers/net/wireless/ath/ath11k/reg.c | 14 +-
drivers/net/wireless/ath/ath11k/reg.h | 4 +-
drivers/net/wireless/ath/ath12k/acpi.c | 2 +
drivers/net/wireless/ath/ath12k/ce.h | 6 +-
drivers/net/wireless/ath/ath12k/core.c | 7 +-
drivers/net/wireless/ath/ath12k/dp.c | 18 +-
drivers/net/wireless/ath/ath12k/dp.h | 1 +
drivers/net/wireless/ath/ath12k/dp_rx.c | 67 +-
drivers/net/wireless/ath/ath12k/dp_tx.c | 47 +-
drivers/net/wireless/ath/ath12k/hal_desc.h | 48 +-
drivers/net/wireless/ath/ath12k/hw.c | 8 +-
drivers/net/wireless/ath/ath12k/hw.h | 3 +-
drivers/net/wireless/ath/ath12k/mac.c | 17 +-
drivers/net/wireless/ath/ath12k/wmi.c | 23 +-
drivers/net/wireless/ath/ath12k/wmi.h | 12 +-
.../broadcom/brcm80211/brcmsmac/phy/phy_lcn.c | 18 +-
drivers/net/wireless/intel/iwlwifi/mvm/link.c | 9 +
drivers/net/wireless/intel/iwlwifi/mvm/mac80211.c | 10 +-
drivers/net/wireless/intel/iwlwifi/mvm/mvm.h | 9 +-
.../net/wireless/intel/iwlwifi/mvm/time-event.c | 5 +-
drivers/net/wireless/marvell/mwifiex/cfg80211.c | 2 +
drivers/net/wireless/realtek/rtl8xxxu/8188f.c | 15 +
drivers/net/wireless/realtek/rtw88/mac.c | 9 +
drivers/net/wireless/realtek/rtw88/main.h | 2 +
drivers/net/wireless/realtek/rtw88/reg.h | 1 +
drivers/net/wireless/realtek/rtw88/rtw8703b.c | 1 +
drivers/net/wireless/realtek/rtw88/rtw8723d.c | 1 +
drivers/net/wireless/realtek/rtw88/rtw8821c.c | 1 +
drivers/net/wireless/realtek/rtw88/rtw8822b.c | 1 +
drivers/net/wireless/realtek/rtw88/rtw8822c.c | 1 +
drivers/net/wireless/realtek/rtw88/usb.c | 6 +-
drivers/net/wireless/realtek/rtw89/debug.c | 2 +-
drivers/net/wireless/realtek/rtw89/fw.c | 13 +-
drivers/net/wireless/realtek/rtw89/mac.c | 5 +-
drivers/net/wireless/realtek/rtw89/pci.c | 23 +-
drivers/net/wireless/realtek/rtw89/rtw8852b.c | 6 +-
drivers/net/wireless/realtek/rtw89/rtw8852b_rfk.c | 2 +-
drivers/net/wireless/virtual/virt_wifi.c | 20 +-
drivers/nvme/host/pci.c | 5 +-
drivers/nvme/target/auth.c | 14 +-
drivers/nvmem/rockchip-otp.c | 1 +
drivers/opp/core.c | 6 +-
drivers/opp/ti-opp-supply.c | 6 +-
drivers/parport/procfs.c | 24 +-
drivers/pci/controller/dwc/pci-keystone.c | 156 +++--
drivers/pci/controller/dwc/pcie-designware-ep.c | 13 +-
drivers/pci/controller/dwc/pcie-dw-rockchip.c | 2 +-
drivers/pci/controller/dwc/pcie-qcom-ep.c | 6 -
drivers/pci/controller/dwc/pcie-tegra194.c | 1 +
drivers/pci/controller/pci-hyperv.c | 4 +-
drivers/pci/controller/pci-loongson.c | 13 +
drivers/pci/controller/pcie-rcar-host.c | 6 +-
drivers/pci/controller/pcie-rockchip.c | 2 +-
drivers/pci/endpoint/functions/pci-epf-test.c | 14 +-
drivers/pci/endpoint/functions/pci-epf-vntb.c | 19 +-
drivers/pci/pci.c | 6 +-
drivers/pci/setup-bus.c | 6 +-
drivers/perf/arm_pmuv3.c | 10 +-
drivers/phy/cadence/phy-cadence-torrent.c | 3 +
drivers/phy/qualcomm/phy-qcom-qmp-pcie.c | 9 +-
drivers/phy/rockchip/Kconfig | 2 +
drivers/phy/xilinx/phy-zynqmp.c | 14 +-
drivers/pinctrl/core.c | 12 +-
drivers/pinctrl/freescale/pinctrl-mxs.c | 4 +-
drivers/pinctrl/pinctrl-rockchip.c | 17 +-
drivers/pinctrl/pinctrl-single.c | 7 +-
drivers/pinctrl/renesas/pfc-r8a779g0.c | 716 ++++++++++-----------
drivers/pinctrl/ti/pinctrl-ti-iodelay.c | 11 +-
drivers/platform/Makefile | 2 +-
drivers/platform/chrome/cros_ec_debugfs.c | 1 +
drivers/platform/mips/cpu_hwmon.c | 3 +
drivers/platform/x86/asus-wmi.c | 6 +-
drivers/power/supply/ab8500_charger.c | 16 +-
drivers/power/supply/ingenic-battery.c | 10 +-
drivers/pwm/pwm-atmel-tcb.c | 12 +-
drivers/pwm/pwm-stm32.c | 5 +-
drivers/remoteproc/imx_rproc.c | 10 +-
drivers/remoteproc/mtk_scp.c | 21 +-
drivers/remoteproc/stm32_rproc.c | 2 +-
drivers/remoteproc/ti_k3_r5_remoteproc.c | 13 +-
drivers/rtc/interface.c | 9 +-
drivers/rtc/rtc-abx80x.c | 12 +-
drivers/rtc/rtc-cmos.c | 10 +-
drivers/rtc/rtc-isl1208.c | 11 +-
drivers/rtc/rtc-tps6594.c | 4 -
drivers/s390/block/dasd_devmap.c | 10 +-
drivers/scsi/lpfc/lpfc_attr.c | 5 +
drivers/scsi/lpfc/lpfc_hbadisc.c | 2 +-
drivers/scsi/lpfc/lpfc_sli.c | 19 +-
drivers/scsi/qla2xxx/qla_bsg.c | 98 +--
drivers/scsi/qla2xxx/qla_def.h | 17 +-
drivers/scsi/qla2xxx/qla_gbl.h | 6 +-
drivers/scsi/qla2xxx/qla_gs.c | 473 +++++++-------
drivers/scsi/qla2xxx/qla_init.c | 92 ++-
drivers/scsi/qla2xxx/qla_inline.h | 8 +
drivers/scsi/qla2xxx/qla_mid.c | 2 +-
drivers/scsi/qla2xxx/qla_nvme.c | 5 +-
drivers/scsi/qla2xxx/qla_os.c | 19 +-
drivers/scsi/qla2xxx/qla_sup.c | 108 +++-
drivers/scsi/sr_ioctl.c | 2 +-
drivers/soc/mediatek/mtk-mutex.c | 1 +
drivers/soc/qcom/icc-bwmon.c | 4 +-
drivers/soc/qcom/pdr_interface.c | 8 +-
drivers/soc/qcom/pmic_glink.c | 13 +-
drivers/soc/qcom/rpmh-rsc.c | 7 +-
drivers/soc/qcom/rpmh.c | 1 -
drivers/soc/qcom/socinfo.c | 3 +-
drivers/soc/xilinx/xlnx_event_manager.c | 15 +-
drivers/soc/xilinx/zynqmp_power.c | 4 +-
drivers/spi/atmel-quadspi.c | 11 +-
drivers/spi/spi-microchip-core.c | 139 ++--
drivers/spi/spidev.c | 1 +
drivers/thermal/broadcom/bcm2835_thermal.c | 19 +-
drivers/thermal/thermal_core.c | 89 ++-
drivers/thermal/thermal_core.h | 10 +-
drivers/ufs/core/ufs-mcq.c | 10 +-
drivers/usb/host/xhci-pci.c | 4 +-
drivers/usb/typec/mux/nb7vpq904m.c | 7 +-
drivers/usb/typec/mux/ptn36502.c | 11 +-
drivers/vhost/vsock.c | 4 +-
drivers/video/fbdev/vesafb.c | 2 +-
drivers/watchdog/rzg2l_wdt.c | 22 +-
fs/btrfs/compression.c | 2 +-
fs/ceph/super.c | 3 +-
fs/erofs/zutil.c | 3 +
fs/exfat/dir.c | 2 +-
fs/ext2/balloc.c | 11 +-
fs/ext4/extents_status.c | 2 +
fs/ext4/fast_commit.c | 6 +
fs/ext4/namei.c | 73 ++-
fs/ext4/xattr.c | 6 +
fs/f2fs/checkpoint.c | 10 +-
fs/f2fs/data.c | 10 +-
fs/f2fs/f2fs.h | 19 +-
fs/f2fs/file.c | 47 +-
fs/f2fs/gc.c | 13 +-
fs/f2fs/inline.c | 8 +-
fs/f2fs/inode.c | 14 +-
fs/f2fs/segment.c | 6 +-
fs/f2fs/segment.h | 3 +-
fs/fuse/inode.c | 24 +-
fs/hfs/inode.c | 3 +
fs/hfsplus/bfind.c | 15 +-
fs/hfsplus/extents.c | 9 +-
fs/hfsplus/hfsplus_fs.h | 21 +
fs/hostfs/hostfs.h | 7 +-
fs/hostfs/hostfs_kern.c | 10 +-
fs/hostfs/hostfs_user.c | 7 +-
fs/jbd2/commit.c | 2 +-
fs/jbd2/journal.c | 56 +-
fs/jbd2/transaction.c | 45 +-
fs/jfs/jfs_imap.c | 5 +-
fs/netfs/write_issue.c | 1 +
fs/nfs/file.c | 5 +-
fs/nfs/nfs4client.c | 6 +-
fs/nfs/nfs4proc.c | 2 +-
fs/nfs/nfstrace.h | 36 +-
fs/nfs/read.c | 8 +-
fs/nfs/write.c | 10 +-
fs/nfsd/Kconfig | 2 +-
fs/nfsd/filecache.c | 2 +-
fs/nfsd/nfs4proc.c | 5 +-
fs/nfsd/nfs4recover.c | 4 +-
fs/nilfs2/btnode.c | 25 +-
fs/nilfs2/btree.c | 4 +-
fs/nilfs2/segment.c | 2 +-
fs/ntfs3/attrib.c | 30 +-
fs/ntfs3/bitmap.c | 2 +-
fs/ntfs3/dir.c | 3 +-
fs/ntfs3/file.c | 5 +-
fs/ntfs3/frecord.c | 2 +-
fs/ntfs3/fslog.c | 5 +-
fs/ntfs3/index.c | 4 +-
fs/ntfs3/inode.c | 13 +-
fs/ntfs3/ntfs.h | 12 +-
fs/ntfs3/super.c | 4 +-
fs/proc/proc_sysctl.c | 6 +-
fs/proc/task_mmu.c | 30 +-
fs/smb/client/cifsfs.c | 8 +-
fs/smb/client/connect.c | 24 +-
fs/super.c | 11 +
fs/udf/balloc.c | 15 +-
fs/udf/file.c | 2 +
fs/udf/inode.c | 11 +-
fs/udf/namei.c | 2 -
fs/udf/super.c | 3 +-
include/asm-generic/vmlinux.lds.h | 2 +-
include/drm/drm_mipi_dsi.h | 46 +-
include/linux/alloc_tag.h | 2 +-
include/linux/bpf_verifier.h | 2 +-
include/linux/firewire.h | 5 +-
include/linux/huge_mm.h | 12 +-
include/linux/hugetlb.h | 1 +
include/linux/interrupt.h | 2 +-
include/linux/jbd2.h | 12 +-
include/linux/lsm_hook_defs.h | 1 +
include/linux/mlx5/qp.h | 9 +-
include/linux/mm.h | 16 +-
include/linux/objagg.h | 1 -
include/linux/perf_event.h | 1 +
include/linux/pgalloc_tag.h | 7 +-
include/linux/preempt.h | 41 ++
include/linux/sbitmap.h | 5 +
include/linux/sched.h | 41 --
include/linux/screen_info.h | 10 +
include/linux/spinlock.h | 14 +-
include/linux/task_work.h | 3 +-
include/linux/virtio_net.h | 11 +
include/net/bluetooth/hci_core.h | 4 -
include/net/ip6_route.h | 22 +-
include/net/ip_fib.h | 1 +
include/net/mana/mana.h | 2 +
include/net/tcp.h | 1 +
include/net/xfrm.h | 36 +-
include/sound/tas2781-dsp.h | 11 +-
include/trace/events/rpcgss.h | 2 +-
include/uapi/drm/xe_drm.h | 8 +-
include/uapi/linux/if_xdp.h | 4 +
include/uapi/linux/netfilter/nf_tables.h | 2 +-
include/uapi/linux/zorro_ids.h | 3 +
include/ufs/ufshcd.h | 6 +
io_uring/io-wq.c | 10 +-
io_uring/io_uring.c | 5 +-
io_uring/napi.c | 2 +
io_uring/opdef.c | 8 +
io_uring/opdef.h | 4 +-
io_uring/register.c | 2 +-
io_uring/timeout.c | 2 +-
io_uring/uring_cmd.c | 2 +-
kernel/bpf/btf.c | 10 +-
kernel/bpf/helpers.c | 2 +-
kernel/bpf/verifier.c | 5 +-
kernel/cgroup/cpuset.c | 76 ++-
kernel/debug/kdb/kdb_io.c | 6 +-
kernel/dma/mapping.c | 2 +-
kernel/events/core.c | 77 ++-
kernel/events/internal.h | 2 +-
kernel/events/ring_buffer.c | 4 +-
kernel/irq/irqdomain.c | 7 +-
kernel/irq/manage.c | 2 +-
kernel/jump_label.c | 45 +-
kernel/locking/rwsem.c | 6 +-
kernel/rcu/tasks.h | 10 +
kernel/sched/core.c | 37 +-
kernel/sched/fair.c | 7 +-
kernel/sched/sched.h | 2 +-
kernel/signal.c | 8 +
kernel/task_work.c | 34 +-
kernel/time/tick-broadcast.c | 23 +
kernel/time/timer_migration.c | 33 +-
kernel/time/timer_migration.h | 12 +-
kernel/trace/pid_list.c | 4 +-
kernel/watchdog_perf.c | 11 +-
kernel/workqueue.c | 6 +-
lib/decompress_bunzip2.c | 3 +-
lib/kobject_uevent.c | 17 +-
lib/objagg.c | 18 +-
lib/sbitmap.c | 36 +-
mm/huge_memory.c | 14 +-
mm/hugetlb.c | 49 +-
mm/memory.c | 2 +-
mm/mempolicy.c | 18 +-
mm/mmap_lock.c | 175 +----
mm/page_alloc.c | 35 +-
mm/vmscan.c | 83 ++-
net/bluetooth/hci_core.c | 27 +-
net/bluetooth/hci_event.c | 2 +
net/bluetooth/hci_sync.c | 2 -
net/bridge/br_forward.c | 4 +-
net/core/filter.c | 15 +-
net/core/flow_dissector.c | 2 +-
net/core/page_pool.c | 2 +-
net/core/xdp.c | 4 +-
net/ethtool/pse-pd.c | 8 +-
net/ipv4/esp4.c | 3 +-
net/ipv4/esp4_offload.c | 7 +
net/ipv4/fib_semantics.c | 13 +-
net/ipv4/fib_trie.c | 1 +
net/ipv4/nexthop.c | 7 +-
net/ipv4/route.c | 18 +-
net/ipv4/tcp.c | 8 +-
net/ipv4/tcp_input.c | 32 +-
net/ipv4/tcp_ipv4.c | 11 +-
net/ipv4/tcp_minisocks.c | 15 +-
net/ipv4/tcp_timer.c | 6 +-
net/ipv6/addrconf.c | 3 +-
net/ipv6/esp6.c | 3 +-
net/ipv6/esp6_offload.c | 7 +
net/ipv6/ip6_output.c | 1 +
net/ipv6/route.c | 2 +-
net/ipv6/tcp_ipv6.c | 10 +-
net/mac80211/chan.c | 11 +
net/mac80211/main.c | 2 +-
net/mac80211/mlme.c | 15 +-
net/mac80211/sta_info.h | 6 +
net/mac80211/tx.c | 6 +-
net/netfilter/ipvs/ip_vs_ctl.c | 10 +-
net/netfilter/ipvs/ip_vs_proto_sctp.c | 4 +-
net/netfilter/nf_conntrack_netlink.c | 3 +-
net/netfilter/nft_set_pipapo.c | 4 +-
net/netfilter/nft_set_pipapo.h | 21 +
net/netfilter/nft_set_pipapo_avx2.c | 22 +-
net/packet/af_packet.c | 86 ++-
net/smc/smc_core.c | 5 +-
net/sunrpc/auth_gss/gss_krb5_keys.c | 2 +-
net/sunrpc/clnt.c | 3 +-
net/sunrpc/xprtrdma/frwr_ops.c | 3 +-
net/sunrpc/xprtrdma/verbs.c | 16 +-
net/tipc/udp_media.c | 5 +-
net/unix/af_unix.c | 41 +-
net/unix/unix_bpf.c | 3 +
net/wireless/nl80211.c | 3 +
net/wireless/util.c | 8 +-
net/xdp/xdp_umem.c | 9 +-
net/xfrm/xfrm_input.c | 8 +-
net/xfrm/xfrm_policy.c | 5 +-
net/xfrm/xfrm_state.c | 65 +-
net/xfrm/xfrm_user.c | 1 -
scripts/Kconfig.include | 3 +-
scripts/Makefile.lib | 6 +-
scripts/gcc-x86_32-has-stack-protector.sh | 2 +-
scripts/gcc-x86_64-has-stack-protector.sh | 2 +-
scripts/syscalltbl.sh | 18 +-
security/apparmor/lsm.c | 7 +
security/apparmor/policy.c | 2 +-
security/apparmor/policy_unpack.c | 43 +-
security/keys/keyctl.c | 2 +-
security/landlock/cred.c | 11 +-
security/security.c | 70 +-
security/selinux/hooks.c | 28 +-
security/smack/smack_lsm.c | 31 +-
sound/core/ump.c | 13 +
sound/firewire/amdtp-stream.c | 3 +-
sound/pci/hda/patch_realtek.c | 6 +-
sound/soc/amd/acp-es8336.c | 4 +-
sound/soc/amd/yc/acp6x-mach.c | 7 +
sound/soc/codecs/cs35l56-shared.c | 2 +-
sound/soc/codecs/max98088.c | 10 +-
sound/soc/codecs/pcm6240.c | 6 +-
sound/soc/codecs/tas2781-fmwlib.c | 20 +-
sound/soc/codecs/tas2781-i2c.c | 39 +-
sound/soc/codecs/wcd939x.c | 113 ++--
sound/soc/fsl/fsl_qmc_audio.c | 2 +
sound/soc/intel/common/soc-acpi-intel-ssp-common.c | 9 +
sound/soc/intel/common/soc-intel-quirks.h | 2 +-
sound/soc/qcom/lpass-cpu.c | 4 +
sound/soc/sof/amd/pci-vangogh.c | 1 -
sound/soc/sof/imx/imx8m.c | 2 +-
sound/soc/sof/intel/hda-loader.c | 18 +-
sound/soc/sof/intel/hda.c | 17 +-
sound/soc/sof/ipc4-topology.c | 46 +-
sound/usb/mixer.c | 7 +
sound/usb/quirks.c | 4 +
tools/bpf/bpftool/common.c | 2 +-
tools/bpf/bpftool/prog.c | 4 +
tools/bpf/resolve_btfids/main.c | 2 +-
tools/lib/bpf/btf.c | 2 +-
tools/lib/bpf/btf_dump.c | 8 +-
tools/lib/bpf/libbpf_internal.h | 10 +-
tools/lib/bpf/linker.c | 11 +-
tools/memory-model/lock.cat | 20 +-
tools/objtool/noreturns.h | 4 +
tools/perf/arch/powerpc/util/skip-callchain-idx.c | 8 +-
tools/perf/arch/x86/util/intel-pt.c | 15 +-
tools/perf/tests/pmu.c | 177 +++++
tools/perf/tests/shell/test_arm_callgraph_fp.sh | 27 +-
tools/perf/tests/workloads/leafloop.c | 20 +-
tools/perf/ui/gtk/annotate.c | 5 +-
tools/perf/util/cs-etm.c | 10 +-
tools/perf/util/disasm.c | 10 +-
tools/perf/util/dso.c | 14 +-
tools/perf/util/dso.h | 19 +
tools/perf/util/maps.c | 9 +-
tools/perf/util/pmu.c | 2 +-
tools/perf/util/pmus.c | 5 +-
tools/perf/util/sort.c | 2 +-
tools/perf/util/srcline.c | 12 +-
tools/perf/util/stat-display.c | 3 +
tools/perf/util/stat-shadow.c | 7 +
tools/perf/util/symbol.c | 18 +-
tools/perf/util/unwind-libdw.c | 12 +-
tools/perf/util/unwind-libunwind-local.c | 18 +-
tools/testing/selftests/bpf/DENYLIST.aarch64 | 1 -
tools/testing/selftests/bpf/bpf_kfuncs.h | 2 +-
.../testing/selftests/bpf/prog_tests/bpf_tcp_ca.c | 16 +-
.../testing/selftests/bpf/prog_tests/fexit_sleep.c | 8 +-
tools/testing/selftests/bpf/prog_tests/sk_lookup.c | 2 +-
.../selftests/bpf/prog_tests/xdp_adjust_tail.c | 2 +-
.../bpf/progs/btf_dump_test_case_multidim.c | 4 +-
.../bpf/progs/btf_dump_test_case_syntax.c | 4 +-
.../bpf/progs/kprobe_multi_session_cookie.c | 2 +-
tools/testing/selftests/bpf/test_sockmap.c | 9 +-
tools/testing/selftests/damon/access_memory.c | 2 +-
.../drivers/net/mlxsw/spectrum-2/tc_flower.sh | 55 +-
tools/testing/selftests/iommu/iommufd.c | 76 ++-
tools/testing/selftests/iommu/iommufd_utils.h | 6 +-
tools/testing/selftests/landlock/base_test.c | 74 +++
tools/testing/selftests/landlock/config | 1 +
tools/testing/selftests/net/fib_tests.sh | 24 +-
.../net/forwarding/bridge_fdb_learning_limit.sh | 18 +
.../selftests/net/forwarding/devlink_lib.sh | 2 +
tools/testing/selftests/nolibc/nolibc-test.c | 2 +-
tools/testing/selftests/resctrl/resctrl_val.c | 54 +-
.../selftests/sigaltstack/current_stack_pointer.h | 2 +-
860 files changed, 7695 insertions(+), 4547 deletions(-)
8 months, 2 weeks
- 15
- 838
[PATCH 6.10.y 0/8] arm64: errata: Speculative SSBS workaround
by Mark Rutland
Hi,
This series is a v6.10-only backport (based on v6.10.3) of the upstream
workaround for SSBS errata on Arm Ltd CPUs, as affected parts are likely to be
used with stable kernels. This does not apply to earlier stable trees, which
will receive a separate backport.
The errata mean that an MSR to the SSBS special-purpose register does not
affect subsequent speculative instructions, permitting speculative store
bypassing for a window of time.
The upstream support was original posted as:
* https://lore.kernel.org/linux-arm-kernel/20240508081400.235362-1-mark.rutla…
"arm64: errata: Add workaround for Arm errata 3194386 and 3312417"
Present in v6.10
* https://lore.kernel.org/linux-arm-kernel/20240603111812.1514101-1-mark.rutl…
"arm64: errata: Expand speculative SSBS workaround"
Present in v6.11-rc1
* https://lore.kernel.org/linux-arm-kernel/20240801101803.1982459-1-mark.rutl…
"arm64: errata: Expand speculative SSBS workaround (again)"
Present in v6.11-rc2
This backport applies the patches which are not present in v6.10.y.
I have tested the backport (when applied to v6.10.3), ensuring that the
detection logic works and that the HWCAP and string in /proc/cpuinfo are
both hidden when the relevant errata are detected.
Mark.
Mark Rutland (8):
arm64: cputype: Add Cortex-X3 definitions
arm64: cputype: Add Cortex-A720 definitions
arm64: cputype: Add Cortex-X925 definitions
arm64: errata: Unify speculative SSBS errata logic
arm64: errata: Expand speculative SSBS workaround
arm64: cputype: Add Cortex-X1C definitions
arm64: cputype: Add Cortex-A725 definitions
arm64: errata: Expand speculative SSBS workaround (again)
Documentation/arch/arm64/silicon-errata.rst | 34 ++++++++++-
arch/arm64/Kconfig | 62 ++++++++++-----------
arch/arm64/include/asm/cpucaps.h | 2 +-
arch/arm64/include/asm/cputype.h | 10 ++++
arch/arm64/kernel/cpu_errata.c | 26 ++++++---
arch/arm64/kernel/proton-pack.c | 2 +-
6 files changed, 93 insertions(+), 43 deletions(-)
--
2.30.2
8 months, 2 weeks
- 3
- 11
[PATCH AUTOSEL 6.10 01/16] regmap: kunit: Fix memory leaks in gen_regmap() and gen_raw_regmap()
by Sasha Levin
From: Richard Fitzgerald <rf(a)opensource.cirrus.com>
[ Upstream commit c3820641da87442251e0c00b6874ef1022da8f58 ]
- Use kunit_kcalloc() to allocate the defaults table so that it will be
freed when the test case ends.
- kfree() the buf and *data buffers on the error paths.
- Use kunit_add_action_or_reset() instead of kunit_add_action() so that
if it fails it will call regmap_exit().
Signed-off-by: Richard Fitzgerald <rf(a)opensource.cirrus.com>
Link: https://msgid.link/r/20240411103724.54063-1-rf@opensource.cirrus.com
Signed-off-by: Mark Brown <broonie(a)kernel.org>
Signed-off-by: Sasha Levin <sashal(a)kernel.org>
---
drivers/base/regmap/regmap-kunit.c | 72 +++++++++++++++++++-----------
1 file changed, 45 insertions(+), 27 deletions(-)
diff --git a/drivers/base/regmap/regmap-kunit.c b/drivers/base/regmap/regmap-kunit.c
index be32cd4e84da4..292e86f601978 100644
--- a/drivers/base/regmap/regmap-kunit.c
+++ b/drivers/base/regmap/regmap-kunit.c
@@ -145,9 +145,9 @@ static struct regmap *gen_regmap(struct kunit *test,
const struct regmap_test_param *param = test->param_value;
struct regmap_test_priv *priv = test->priv;
unsigned int *buf;
- struct regmap *ret;
+ struct regmap *ret = ERR_PTR(-ENOMEM);
size_t size;
- int i;
+ int i, error;
struct reg_default *defaults;
config->cache_type = param->cache;
@@ -172,15 +172,17 @@ static struct regmap *gen_regmap(struct kunit *test,
*data = kzalloc(sizeof(**data), GFP_KERNEL);
if (!(*data))
- return ERR_PTR(-ENOMEM);
+ goto out_free;
(*data)->vals = buf;
if (config->num_reg_defaults) {
- defaults = kcalloc(config->num_reg_defaults,
- sizeof(struct reg_default),
- GFP_KERNEL);
+ defaults = kunit_kcalloc(test,
+ config->num_reg_defaults,
+ sizeof(struct reg_default),
+ GFP_KERNEL);
if (!defaults)
- return ERR_PTR(-ENOMEM);
+ goto out_free;
+
config->reg_defaults = defaults;
for (i = 0; i < config->num_reg_defaults; i++) {
@@ -190,12 +192,19 @@ static struct regmap *gen_regmap(struct kunit *test,
}
ret = regmap_init_ram(priv->dev, config, *data);
- if (IS_ERR(ret)) {
- kfree(buf);
- kfree(*data);
- } else {
- kunit_add_action(test, regmap_exit_action, ret);
- }
+ if (IS_ERR(ret))
+ goto out_free;
+
+ /* This calls regmap_exit() on failure, which frees buf and *data */
+ error = kunit_add_action_or_reset(test, regmap_exit_action, ret);
+ if (error)
+ ret = ERR_PTR(error);
+
+ return ret;
+
+out_free:
+ kfree(buf);
+ kfree(*data);
return ret;
}
@@ -1497,9 +1506,9 @@ static struct regmap *gen_raw_regmap(struct kunit *test,
struct regmap_test_priv *priv = test->priv;
const struct regmap_test_param *param = test->param_value;
u16 *buf;
- struct regmap *ret;
+ struct regmap *ret = ERR_PTR(-ENOMEM);
size_t size = (config->max_register + 1) * config->reg_bits / 8;
- int i;
+ int i, error;
struct reg_default *defaults;
config->cache_type = param->cache;
@@ -1515,15 +1524,16 @@ static struct regmap *gen_raw_regmap(struct kunit *test,
*data = kzalloc(sizeof(**data), GFP_KERNEL);
if (!(*data))
- return ERR_PTR(-ENOMEM);
+ goto out_free;
(*data)->vals = (void *)buf;
config->num_reg_defaults = config->max_register + 1;
- defaults = kcalloc(config->num_reg_defaults,
- sizeof(struct reg_default),
- GFP_KERNEL);
+ defaults = kunit_kcalloc(test,
+ config->num_reg_defaults,
+ sizeof(struct reg_default),
+ GFP_KERNEL);
if (!defaults)
- return ERR_PTR(-ENOMEM);
+ goto out_free;
config->reg_defaults = defaults;
for (i = 0; i < config->num_reg_defaults; i++) {
@@ -1536,7 +1546,8 @@ static struct regmap *gen_raw_regmap(struct kunit *test,
defaults[i].def = be16_to_cpu(buf[i]);
break;
default:
- return ERR_PTR(-EINVAL);
+ ret = ERR_PTR(-EINVAL);
+ goto out_free;
}
}
@@ -1548,12 +1559,19 @@ static struct regmap *gen_raw_regmap(struct kunit *test,
config->num_reg_defaults = 0;
ret = regmap_init_raw_ram(priv->dev, config, *data);
- if (IS_ERR(ret)) {
- kfree(buf);
- kfree(*data);
- } else {
- kunit_add_action(test, regmap_exit_action, ret);
- }
+ if (IS_ERR(ret))
+ goto out_free;
+
+ /* This calls regmap_exit() on failure, which frees buf and *data */
+ error = kunit_add_action_or_reset(test, regmap_exit_action, ret);
+ if (error)
+ ret = ERR_PTR(error);
+
+ return ret;
+
+out_free:
+ kfree(buf);
+ kfree(*data);
return ret;
}
--
2.43.0
8 months, 2 weeks
- 5
- 21
FAILED: patch "[PATCH] mptcp: pm: do not ignore 'subflow' if 'signal' flag is also" failed to apply to 6.1-stable tree
by gregkh＠linuxfoundation.org
The patch below does not apply to the 6.1-stable tree.
If someone wants it applied there, or to any other stable or longterm
tree, then please email the backport, including the original git commit
id to <stable(a)vger.kernel.org>.
To reproduce the conflict and resubmit, you may use the following commands:
git fetch https://git.kernel.org/pub/scm/linux/kernel/git/stable/linux.git/ linux-6.1.y
git checkout FETCH_HEAD
git cherry-pick -x 85df533a787bf07bf4367ce2a02b822ff1fba1a3
# <resolve conflicts, build, test, etc.>
git commit -s
git send-email --to '<stable(a)vger.kernel.org>' --in-reply-to '2024081200-squiggle-idly-2e63@gregkh' --subject-prefix 'PATCH 6.1.y' HEAD^..
Possible dependencies:
85df533a787b ("mptcp: pm: do not ignore 'subflow' if 'signal' flag is also set")
c95eb32ced82 ("mptcp: pm: reduce indentation blocks")
528cb5f2a1e8 ("mptcp: pass addr to mptcp_pm_alloc_anno_list")
77e4b94a3de6 ("mptcp: update userspace pm infos")
24430f8bf516 ("mptcp: add address into userspace pm list")
fb00ee4f3343 ("mptcp: netlink: respect v4/v6-only sockets")
80638684e840 ("mptcp: get sk from msk directly")
thanks,
greg k-h
------------------ original commit in Linus's tree ------------------
From 85df533a787bf07bf4367ce2a02b822ff1fba1a3 Mon Sep 17 00:00:00 2001
From: "Matthieu Baerts (NGI0)" <matttbe(a)kernel.org>
Date: Wed, 31 Jul 2024 13:05:57 +0200
Subject: [PATCH] mptcp: pm: do not ignore 'subflow' if 'signal' flag is also
set
Up to the 'Fixes' commit, having an endpoint with both the 'signal' and
'subflow' flags, resulted in the creation of a subflow and an address
announcement using the address linked to this endpoint. After this
commit, only the address announcement was done, ignoring the 'subflow'
flag.
That's because the same bitmap is used for the two flags. It is OK to
keep this single bitmap, the already selected local endpoint simply have
to be re-used, but not via select_local_address() not to look at the
just modified bitmap.
Note that it is unusual to set the two flags together: creating a new
subflow using a new local address will implicitly advertise it to the
other peer. So in theory, no need to advertise it explicitly as well.
Maybe there are use-cases -- the subflow might not reach the other peer
that way, we can ask the other peer to try initiating the new subflow
without delay -- or very likely the user is confused, and put both flags
"just to be sure at least the right one is set". Still, if it is
allowed, the kernel should do what has been asked: using this endpoint
to announce the address and to create a new subflow from it.
An alternative is to forbid the use of the two flags together, but
that's probably too late, there are maybe use-cases, and it was working
before. This patch will avoid people complaining subflows are not
created using the endpoint they added with the 'subflow' and 'signal'
flag.
Note that with the current patch, the subflow might not be created in
some corner cases, e.g. if the 'subflows' limit was reached when sending
the ADD_ADDR, but changed later on. It is probably not worth splitting
id_avail_bitmap per target ('signal', 'subflow'), which will add another
large field to the msk "just" to track (again) endpoints. Anyway,
currently when the limits are changed, the kernel doesn't check if new
subflows can be created or removed, because we would need to keep track
of the received ADD_ADDR, and more. It sounds OK to assume that the
limits should be properly configured before establishing new
connections.
Fixes: 86e39e04482b ("mptcp: keep track of local endpoint still available for each msk")
Cc: stable(a)vger.kernel.org
Suggested-by: Paolo Abeni <pabeni(a)redhat.com>
Reviewed-by: Mat Martineau <martineau(a)kernel.org>
Signed-off-by: Matthieu Baerts (NGI0) <matttbe(a)kernel.org>
Link: https://patch.msgid.link/20240731-upstream-net-20240731-mptcp-endp-subflow-…
Signed-off-by: Jakub Kicinski <kuba(a)kernel.org>
diff --git a/net/mptcp/pm_netlink.c b/net/mptcp/pm_netlink.c
index 2be7af377cda..4cae2aa7be5c 100644
--- a/net/mptcp/pm_netlink.c
+++ b/net/mptcp/pm_netlink.c
@@ -512,8 +512,8 @@ __lookup_addr(struct pm_nl_pernet *pernet, const struct mptcp_addr_info *info)
static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
{
+ struct mptcp_pm_addr_entry *local, *signal_and_subflow = NULL;
struct sock *sk = (struct sock *)msk;
- struct mptcp_pm_addr_entry *local;
unsigned int add_addr_signal_max;
unsigned int local_addr_max;
struct pm_nl_pernet *pernet;
@@ -579,6 +579,9 @@ static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
msk->pm.add_addr_signaled++;
mptcp_pm_announce_addr(msk, &local->addr, false);
mptcp_pm_nl_addr_send_ack(msk);
+
+ if (local->flags & MPTCP_PM_ADDR_FLAG_SUBFLOW)
+ signal_and_subflow = local;
}
subflow:
@@ -589,9 +592,14 @@ static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
bool fullmesh;
int i, nr;
- local = select_local_address(pernet, msk);
- if (!local)
- break;
+ if (signal_and_subflow) {
+ local = signal_and_subflow;
+ signal_and_subflow = NULL;
+ } else {
+ local = select_local_address(pernet, msk);
+ if (!local)
+ break;
+ }
fullmesh = !!(local->flags & MPTCP_PM_ADDR_FLAG_FULLMESH);
8 months, 2 weeks
- 1
- 0
FAILED: patch "[PATCH] mptcp: pm: do not ignore 'subflow' if 'signal' flag is also" failed to apply to 6.6-stable tree
by gregkh＠linuxfoundation.org
The patch below does not apply to the 6.6-stable tree.
If someone wants it applied there, or to any other stable or longterm
tree, then please email the backport, including the original git commit
id to <stable(a)vger.kernel.org>.
To reproduce the conflict and resubmit, you may use the following commands:
git fetch https://git.kernel.org/pub/scm/linux/kernel/git/stable/linux.git/ linux-6.6.y
git checkout FETCH_HEAD
git cherry-pick -x 85df533a787bf07bf4367ce2a02b822ff1fba1a3
# <resolve conflicts, build, test, etc.>
git commit -s
git send-email --to '<stable(a)vger.kernel.org>' --in-reply-to '2024081258-tableware-unclog-6530@gregkh' --subject-prefix 'PATCH 6.6.y' HEAD^..
Possible dependencies:
85df533a787b ("mptcp: pm: do not ignore 'subflow' if 'signal' flag is also set")
c95eb32ced82 ("mptcp: pm: reduce indentation blocks")
thanks,
greg k-h
------------------ original commit in Linus's tree ------------------
From 85df533a787bf07bf4367ce2a02b822ff1fba1a3 Mon Sep 17 00:00:00 2001
From: "Matthieu Baerts (NGI0)" <matttbe(a)kernel.org>
Date: Wed, 31 Jul 2024 13:05:57 +0200
Subject: [PATCH] mptcp: pm: do not ignore 'subflow' if 'signal' flag is also
set
Up to the 'Fixes' commit, having an endpoint with both the 'signal' and
'subflow' flags, resulted in the creation of a subflow and an address
announcement using the address linked to this endpoint. After this
commit, only the address announcement was done, ignoring the 'subflow'
flag.
That's because the same bitmap is used for the two flags. It is OK to
keep this single bitmap, the already selected local endpoint simply have
to be re-used, but not via select_local_address() not to look at the
just modified bitmap.
Note that it is unusual to set the two flags together: creating a new
subflow using a new local address will implicitly advertise it to the
other peer. So in theory, no need to advertise it explicitly as well.
Maybe there are use-cases -- the subflow might not reach the other peer
that way, we can ask the other peer to try initiating the new subflow
without delay -- or very likely the user is confused, and put both flags
"just to be sure at least the right one is set". Still, if it is
allowed, the kernel should do what has been asked: using this endpoint
to announce the address and to create a new subflow from it.
An alternative is to forbid the use of the two flags together, but
that's probably too late, there are maybe use-cases, and it was working
before. This patch will avoid people complaining subflows are not
created using the endpoint they added with the 'subflow' and 'signal'
flag.
Note that with the current patch, the subflow might not be created in
some corner cases, e.g. if the 'subflows' limit was reached when sending
the ADD_ADDR, but changed later on. It is probably not worth splitting
id_avail_bitmap per target ('signal', 'subflow'), which will add another
large field to the msk "just" to track (again) endpoints. Anyway,
currently when the limits are changed, the kernel doesn't check if new
subflows can be created or removed, because we would need to keep track
of the received ADD_ADDR, and more. It sounds OK to assume that the
limits should be properly configured before establishing new
connections.
Fixes: 86e39e04482b ("mptcp: keep track of local endpoint still available for each msk")
Cc: stable(a)vger.kernel.org
Suggested-by: Paolo Abeni <pabeni(a)redhat.com>
Reviewed-by: Mat Martineau <martineau(a)kernel.org>
Signed-off-by: Matthieu Baerts (NGI0) <matttbe(a)kernel.org>
Link: https://patch.msgid.link/20240731-upstream-net-20240731-mptcp-endp-subflow-…
Signed-off-by: Jakub Kicinski <kuba(a)kernel.org>
diff --git a/net/mptcp/pm_netlink.c b/net/mptcp/pm_netlink.c
index 2be7af377cda..4cae2aa7be5c 100644
--- a/net/mptcp/pm_netlink.c
+++ b/net/mptcp/pm_netlink.c
@@ -512,8 +512,8 @@ __lookup_addr(struct pm_nl_pernet *pernet, const struct mptcp_addr_info *info)
static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
{
+ struct mptcp_pm_addr_entry *local, *signal_and_subflow = NULL;
struct sock *sk = (struct sock *)msk;
- struct mptcp_pm_addr_entry *local;
unsigned int add_addr_signal_max;
unsigned int local_addr_max;
struct pm_nl_pernet *pernet;
@@ -579,6 +579,9 @@ static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
msk->pm.add_addr_signaled++;
mptcp_pm_announce_addr(msk, &local->addr, false);
mptcp_pm_nl_addr_send_ack(msk);
+
+ if (local->flags & MPTCP_PM_ADDR_FLAG_SUBFLOW)
+ signal_and_subflow = local;
}
subflow:
@@ -589,9 +592,14 @@ static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
bool fullmesh;
int i, nr;
- local = select_local_address(pernet, msk);
- if (!local)
- break;
+ if (signal_and_subflow) {
+ local = signal_and_subflow;
+ signal_and_subflow = NULL;
+ } else {
+ local = select_local_address(pernet, msk);
+ if (!local)
+ break;
+ }
fullmesh = !!(local->flags & MPTCP_PM_ADDR_FLAG_FULLMESH);
8 months, 2 weeks
- 1
- 0
FAILED: patch "[PATCH] mptcp: pm: do not ignore 'subflow' if 'signal' flag is also" failed to apply to 6.10-stable tree
by gregkh＠linuxfoundation.org
The patch below does not apply to the 6.10-stable tree.
If someone wants it applied there, or to any other stable or longterm
tree, then please email the backport, including the original git commit
id to <stable(a)vger.kernel.org>.
To reproduce the conflict and resubmit, you may use the following commands:
git fetch https://git.kernel.org/pub/scm/linux/kernel/git/stable/linux.git/ linux-6.10.y
git checkout FETCH_HEAD
git cherry-pick -x 85df533a787bf07bf4367ce2a02b822ff1fba1a3
# <resolve conflicts, build, test, etc.>
git commit -s
git send-email --to '<stable(a)vger.kernel.org>' --in-reply-to '2024081257-budding-jeep-9fa3@gregkh' --subject-prefix 'PATCH 6.10.y' HEAD^..
Possible dependencies:
85df533a787b ("mptcp: pm: do not ignore 'subflow' if 'signal' flag is also set")
c95eb32ced82 ("mptcp: pm: reduce indentation blocks")
thanks,
greg k-h
------------------ original commit in Linus's tree ------------------
From 85df533a787bf07bf4367ce2a02b822ff1fba1a3 Mon Sep 17 00:00:00 2001
From: "Matthieu Baerts (NGI0)" <matttbe(a)kernel.org>
Date: Wed, 31 Jul 2024 13:05:57 +0200
Subject: [PATCH] mptcp: pm: do not ignore 'subflow' if 'signal' flag is also
set
Up to the 'Fixes' commit, having an endpoint with both the 'signal' and
'subflow' flags, resulted in the creation of a subflow and an address
announcement using the address linked to this endpoint. After this
commit, only the address announcement was done, ignoring the 'subflow'
flag.
That's because the same bitmap is used for the two flags. It is OK to
keep this single bitmap, the already selected local endpoint simply have
to be re-used, but not via select_local_address() not to look at the
just modified bitmap.
Note that it is unusual to set the two flags together: creating a new
subflow using a new local address will implicitly advertise it to the
other peer. So in theory, no need to advertise it explicitly as well.
Maybe there are use-cases -- the subflow might not reach the other peer
that way, we can ask the other peer to try initiating the new subflow
without delay -- or very likely the user is confused, and put both flags
"just to be sure at least the right one is set". Still, if it is
allowed, the kernel should do what has been asked: using this endpoint
to announce the address and to create a new subflow from it.
An alternative is to forbid the use of the two flags together, but
that's probably too late, there are maybe use-cases, and it was working
before. This patch will avoid people complaining subflows are not
created using the endpoint they added with the 'subflow' and 'signal'
flag.
Note that with the current patch, the subflow might not be created in
some corner cases, e.g. if the 'subflows' limit was reached when sending
the ADD_ADDR, but changed later on. It is probably not worth splitting
id_avail_bitmap per target ('signal', 'subflow'), which will add another
large field to the msk "just" to track (again) endpoints. Anyway,
currently when the limits are changed, the kernel doesn't check if new
subflows can be created or removed, because we would need to keep track
of the received ADD_ADDR, and more. It sounds OK to assume that the
limits should be properly configured before establishing new
connections.
Fixes: 86e39e04482b ("mptcp: keep track of local endpoint still available for each msk")
Cc: stable(a)vger.kernel.org
Suggested-by: Paolo Abeni <pabeni(a)redhat.com>
Reviewed-by: Mat Martineau <martineau(a)kernel.org>
Signed-off-by: Matthieu Baerts (NGI0) <matttbe(a)kernel.org>
Link: https://patch.msgid.link/20240731-upstream-net-20240731-mptcp-endp-subflow-…
Signed-off-by: Jakub Kicinski <kuba(a)kernel.org>
diff --git a/net/mptcp/pm_netlink.c b/net/mptcp/pm_netlink.c
index 2be7af377cda..4cae2aa7be5c 100644
--- a/net/mptcp/pm_netlink.c
+++ b/net/mptcp/pm_netlink.c
@@ -512,8 +512,8 @@ __lookup_addr(struct pm_nl_pernet *pernet, const struct mptcp_addr_info *info)
static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
{
+ struct mptcp_pm_addr_entry *local, *signal_and_subflow = NULL;
struct sock *sk = (struct sock *)msk;
- struct mptcp_pm_addr_entry *local;
unsigned int add_addr_signal_max;
unsigned int local_addr_max;
struct pm_nl_pernet *pernet;
@@ -579,6 +579,9 @@ static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
msk->pm.add_addr_signaled++;
mptcp_pm_announce_addr(msk, &local->addr, false);
mptcp_pm_nl_addr_send_ack(msk);
+
+ if (local->flags & MPTCP_PM_ADDR_FLAG_SUBFLOW)
+ signal_and_subflow = local;
}
subflow:
@@ -589,9 +592,14 @@ static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
bool fullmesh;
int i, nr;
- local = select_local_address(pernet, msk);
- if (!local)
- break;
+ if (signal_and_subflow) {
+ local = signal_and_subflow;
+ signal_and_subflow = NULL;
+ } else {
+ local = select_local_address(pernet, msk);
+ if (!local)
+ break;
+ }
fullmesh = !!(local->flags & MPTCP_PM_ADDR_FLAG_FULLMESH);
8 months, 2 weeks
- 1
- 0
FAILED: patch "[PATCH] mptcp: pm: fix backup support in signal endpoints" failed to apply to 5.10-stable tree
by gregkh＠linuxfoundation.org
The patch below does not apply to the 5.10-stable tree.
If someone wants it applied there, or to any other stable or longterm
tree, then please email the backport, including the original git commit
id to <stable(a)vger.kernel.org>.
To reproduce the conflict and resubmit, you may use the following commands:
git fetch https://git.kernel.org/pub/scm/linux/kernel/git/stable/linux.git/ linux-5.10.y
git checkout FETCH_HEAD
git cherry-pick -x 6834097fc38c5416701c793da94558cea49c0a1f
# <resolve conflicts, build, test, etc.>
git commit -s
git send-email --to '<stable(a)vger.kernel.org>' --in-reply-to '2024080729-unclaimed-shopping-6751@gregkh' --subject-prefix 'PATCH 5.10.y' HEAD^..
Possible dependencies:
6834097fc38c ("mptcp: pm: fix backup support in signal endpoints")
9ae7846c4b6b ("mptcp: dump addrs in userspace pm list")
34e74a5cf3b7 ("mptcp: implement mptcp_userspace_pm_dump_addr")
aab4d8564947 ("net: mptcp: use policy generated by YAML spec")
1e07938e29c5 ("net: mptcp: rename netlink handlers to mptcp_pm_nl_<blah>_{doit,dumpit}")
1d0507f46843 ("net: mptcp: convert netlink from small_ops to ops")
740ebe35bd3f ("mptcp: add struct mptcp_sched_ops")
6ba7ce89905c ("mptcp: unify pm set_flags interfaces")
f40be0db0b76 ("mptcp: unify pm get_flags_and_ifindex_by_id")
a963853fd465 ("mptcp: use net instead of sock_net")
dfc8d0603033 ("mptcp: implement delayed seq generation for passive fastopen")
d15697185404 ("mptcp: allow privileged operations from user namespaces")
9c5d03d36251 ("genetlink: start to validate reserved header bytes")
02739545951a ("net: Fix data-races around sysctl_[rw]mem(_offset)?.")
892f396c8e68 ("mptcp: netlink: issue MP_PRIO signals from userspace PMs")
a657430260e5 ("mptcp: Acquire the subflow socket lock before modifying MP_PRIO flags")
c21b50d5912b ("mptcp: Avoid acquiring PM lock for subflow priority changes")
6f664045c868 ("Merge tag 'mm-nonmm-stable-2022-05-26' of git://git.kernel.org/pub/scm/linux/kernel/git/akpm/mm")
thanks,
greg k-h
------------------ original commit in Linus's tree ------------------
From 6834097fc38c5416701c793da94558cea49c0a1f Mon Sep 17 00:00:00 2001
From: "Matthieu Baerts (NGI0)" <matttbe(a)kernel.org>
Date: Sat, 27 Jul 2024 12:01:28 +0200
Subject: [PATCH] mptcp: pm: fix backup support in signal endpoints
There was a support for signal endpoints, but only when the endpoint's
flag was changed during a connection. If an endpoint with the signal and
backup was already present, the MP_JOIN reply was not containing the
backup flag as expected.
That's confusing to have this inconsistent behaviour. On the other hand,
the infrastructure to set the backup flag in the SYN + ACK + MP_JOIN was
already there, it was just never set before. Now when requesting the
local ID from the path-manager, the backup status is also requested.
Note that when the userspace PM is used, the backup flag can be set if
the local address was already used before with a backup flag, e.g. if
the address was announced with the 'backup' flag, or a subflow was
created with the 'backup' flag.
Fixes: 4596a2c1b7f5 ("mptcp: allow creating non-backup subflows")
Cc: stable(a)vger.kernel.org
Closes: https://github.com/multipath-tcp/mptcp_net-next/issues/507
Reviewed-by: Mat Martineau <martineau(a)kernel.org>
Signed-off-by: Matthieu Baerts (NGI0) <matttbe(a)kernel.org>
Signed-off-by: Paolo Abeni <pabeni(a)redhat.com>
diff --git a/net/mptcp/pm.c b/net/mptcp/pm.c
index 55406720c607..23bb89c94e90 100644
--- a/net/mptcp/pm.c
+++ b/net/mptcp/pm.c
@@ -426,6 +426,18 @@ int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc)
return mptcp_pm_nl_get_local_id(msk, &skc_local);
}
+bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc)
+{
+ struct mptcp_addr_info skc_local;
+
+ mptcp_local_address((struct sock_common *)skc, &skc_local);
+
+ if (mptcp_pm_is_userspace(msk))
+ return mptcp_userspace_pm_is_backup(msk, &skc_local);
+
+ return mptcp_pm_nl_is_backup(msk, &skc_local);
+}
+
int mptcp_pm_get_flags_and_ifindex_by_id(struct mptcp_sock *msk, unsigned int id,
u8 *flags, int *ifindex)
{
diff --git a/net/mptcp/pm_netlink.c b/net/mptcp/pm_netlink.c
index 7635fac91539..37954a0b087d 100644
--- a/net/mptcp/pm_netlink.c
+++ b/net/mptcp/pm_netlink.c
@@ -1101,6 +1101,24 @@ int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk, struct mptcp_addr_info *skc
return ret;
}
+bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc)
+{
+ struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk);
+ struct mptcp_pm_addr_entry *entry;
+ bool backup = false;
+
+ rcu_read_lock();
+ list_for_each_entry_rcu(entry, &pernet->local_addr_list, list) {
+ if (mptcp_addresses_equal(&entry->addr, skc, entry->addr.port)) {
+ backup = !!(entry->flags & MPTCP_PM_ADDR_FLAG_BACKUP);
+ break;
+ }
+ }
+ rcu_read_unlock();
+
+ return backup;
+}
+
#define MPTCP_PM_CMD_GRP_OFFSET 0
#define MPTCP_PM_EV_GRP_OFFSET 1
diff --git a/net/mptcp/pm_userspace.c b/net/mptcp/pm_userspace.c
index f0a4590506c6..8eaa9fbe3e34 100644
--- a/net/mptcp/pm_userspace.c
+++ b/net/mptcp/pm_userspace.c
@@ -165,6 +165,24 @@ int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk,
return mptcp_userspace_pm_append_new_local_addr(msk, &new_entry, true);
}
+bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk,
+ struct mptcp_addr_info *skc)
+{
+ struct mptcp_pm_addr_entry *entry;
+ bool backup = false;
+
+ spin_lock_bh(&msk->pm.lock);
+ list_for_each_entry(entry, &msk->pm.userspace_pm_local_addr_list, list) {
+ if (mptcp_addresses_equal(&entry->addr, skc, false)) {
+ backup = !!(entry->flags & MPTCP_PM_ADDR_FLAG_BACKUP);
+ break;
+ }
+ }
+ spin_unlock_bh(&msk->pm.lock);
+
+ return backup;
+}
+
int mptcp_pm_nl_announce_doit(struct sk_buff *skb, struct genl_info *info)
{
struct nlattr *token = info->attrs[MPTCP_PM_ATTR_TOKEN];
diff --git a/net/mptcp/protocol.h b/net/mptcp/protocol.h
index b8b25124e7de..60c6b073d65f 100644
--- a/net/mptcp/protocol.h
+++ b/net/mptcp/protocol.h
@@ -1109,6 +1109,9 @@ bool mptcp_pm_rm_addr_signal(struct mptcp_sock *msk, unsigned int remaining,
int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
+bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc);
+bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
+bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
int mptcp_pm_dump_addr(struct sk_buff *msg, struct netlink_callback *cb);
int mptcp_pm_nl_dump_addr(struct sk_buff *msg,
struct netlink_callback *cb);
diff --git a/net/mptcp/subflow.c b/net/mptcp/subflow.c
index be406197b1c4..0e4b5bfbeaa1 100644
--- a/net/mptcp/subflow.c
+++ b/net/mptcp/subflow.c
@@ -100,6 +100,7 @@ static struct mptcp_sock *subflow_token_join_request(struct request_sock *req)
return NULL;
}
subflow_req->local_id = local_id;
+ subflow_req->request_bkup = mptcp_pm_is_backup(msk, (struct sock_common *)req);
return msk;
}
@@ -620,6 +621,8 @@ static int subflow_chk_local_id(struct sock *sk)
return err;
subflow_set_local_id(subflow, err);
+ subflow->request_bkup = mptcp_pm_is_backup(msk, (struct sock_common *)sk);
+
return 0;
}
8 months, 2 weeks
- 3
- 3