Linux 6.12.75

DISCUSSION Sasha Levin 3 participants 9 messages Mar 4 – Apr 15

Subsystems (2)

Stable branch Regressions

lore

Share & tools

lore

Sasha Levin

author maintainer

2026-03-04 13:14 UTC #0 lore raw

-----BEGIN PGP SIGNED MESSAGE-----
Hash: SHA512

I'm announcing the release of the 6.12.75 kernel.

All users of the 6.12 kernel series must upgrade.

The updated 6.12.y git tree can be found at:
git://git.kernel.org/pub/scm/linux/kernel/git/stable/linux-stable.git linux-6.12.y
and can be browsed at the normal kernel.org git web browser:
https://git.kernel.org/?p=linux/kernel/git/stable/linux-stable.git;a=summary

Thanks,
Sasha

- ------------

-----BEGIN PGP SIGNATURE-----

iQIzBAEBCgAdFiEE4n5dijQDou9mhzu83qZv95d3LNwFAmmoMBYACgkQ3qZv95d3 LNwN5A//a0R4DF5M/Blyz0BLhBR4JVYcqttz+5x+Sd+RjD+n5HzWwa/8TvGva2HG sKligVyjEVVN7YbSrYhAO+nzM7qH2JoWm/PYHwkumVIOGR5eZ7Mgd31kAZMWSXb+ 6jhrBsys8F1IfjZj2Kaj/jq3cVlLaf7WeGrZdtaASFoNzhDrEBr0tCMEdbVsEiUm oaLd4Ep0hB9pRqN66Xgj8uTpH0E9HPqqgLy1QyX4Fta5XAS11Wm7Bt8tvHilJQvP O6CCNfHM9NTSJ0c612hrBRf8cVJl1X5kYvSYccDCw2Usm6Darl+s43w/RzFt6TtW /WaakJLwAxCizctILYQGdMtBAmuUMp00OIdd/7Vw9aytnXuY/4yi4s26h0jrYgaA ok4BEsIDZ2/r3ZaX9TI6w/se6g1IdD1AwMm8pjaEIGylbIb46NRCPdb6vU0vvqd9 Nz4q+l5std27BLg6hWlh9KbkMeiacdUDyASf8gn9GkaEE+zyU+LhxK4024cwHVbt +lBE7N4+TjT9BYBrdyv7KGEFUGv19E/TuPji91w1DB+gB0UKGb/E1/fPI/ExS0Iu Y1DURBrvT4AtB3Ve9mPkY2YNE34sB0zs/3QOnDb7UGmTJBVbxnzye6qyIERKQUGa LM73p8f2867zVYyj/okgDmVNiTA1uaMg2g6qasXP+oCKrZlCJ2g= =FyPR
-----END PGP SIGNATURE-----

Sasha Levin

author maintainer

2026-03-04 13:14 UTC #1 lore raw

Documentation/PCI/endpoint/pci-vntb-howto.rst +7 -7

index 70d3bc90893f3..949c0d35694c2 100644
@@ -52,14 +52,14 @@ pci-epf-vntb device, the following commands can be used::
 	# cd /sys/kernel/config/pci_ep/
 	# mkdir functions/pci_epf_vntb/func1
 
-The "mkdir func1" above creates the pci-epf-ntb function device that will
+The "mkdir func1" above creates the pci-epf-vntb function device that will
 be probed by pci_epf_vntb driver.
 
 The PCI endpoint framework populates the directory with the following
 configurable fields::
 
-	# ls functions/pci_epf_ntb/func1
-	baseclass_code    deviceid          msi_interrupts    pci-epf-ntb.0
+	# ls functions/pci_epf_vntb/func1
+	baseclass_code    deviceid          msi_interrupts    pci-epf-vntb.0
 	progif_code       secondary         subsys_id         vendorid
 	cache_line_size   interrupt_pin     msix_interrupts   primary
 	revid             subclass_code     subsys_vendor_id

@@ -106,13 +106,13 @@ A sample configuration for virtual NTB driver for virtual PCI bus::
 	# echo 0x080A > functions/pci_epf_vntb/func1/pci_epf_vntb.0/vntb_pid
 	# echo 0x10 > functions/pci_epf_vntb/func1/pci_epf_vntb.0/vbus_number
 
-Binding pci-epf-ntb Device to EP Controller
+Binding pci-epf-vntb Device to EP Controller
 --------------------------------------------
 
 NTB function device should be attached to PCI endpoint controllers
 connected to the host.
 
-	# ln -s controllers/5f010000.pcie_ep functions/pci-epf-ntb/func1/primary
+	# ln -s controllers/5f010000.pcie_ep functions/pci_epf_vntb/func1/primary
 
 Once the above step is completed, the PCI endpoint controllers are ready to
 establish a link with the host.

@@ -134,7 +134,7 @@ lspci Output at Host side
 -------------------------
 
 Note that the devices listed here correspond to the values populated in
-"Creating pci-epf-ntb Device" section above::
+"Creating pci-epf-vntb Device" section above::
 
 	# lspci
         00:00.0 PCI bridge: Freescale Semiconductor Inc Device 0000 (rev 01)

@@ -147,7 +147,7 @@ lspci Output at EP Side / Virtual PCI bus
 -----------------------------------------
 
 Note that the devices listed here correspond to the values populated in
-"Creating pci-epf-ntb Device" section above::
+"Creating pci-epf-vntb Device" section above::
 
         # lspci
         10:00.0 Unassigned class [ffff]: Dawicontrol Computersysteme GmbH Device 1234 (rev ff)

Documentation/devicetree/bindings/phy/qcom,edp-phy.yaml +27 -1

index 4e15d90d08b0e..27d6bbed5da0f 100644
@@ -31,12 +31,15 @@ properties:
       - description: PLL register block
 
   clocks:
-    maxItems: 2
+    minItems: 2
+    maxItems: 3
 
   clock-names:
+    minItems: 2
     items:
       - const: aux
       - const: cfg_ahb
+      - const: ref
 
   "#clock-cells":
     const: 1

@@ -58,6 +61,29 @@ required:
   - "#clock-cells"
   - "#phy-cells"
 
+allOf:
+  - if:
+      properties:
+        compatible:
+          enum:
+            - qcom,x1e80100-dp-phy
+    then:
+      properties:
+        clocks:
+          minItems: 3
+          maxItems: 3
+        clock-names:
+          minItems: 3
+          maxItems: 3
+    else:
+      properties:
+        clocks:
+          minItems: 2
+          maxItems: 2
+        clock-names:
+          minItems: 2
+          maxItems: 2
+
 additionalProperties: false
 
 examples:

Documentation/devicetree/bindings/sound/asahi-kasei,ak4458.yaml +3 -3

index 4477f84b7acc0..e44801ddbd2a9 100644
@@ -18,10 +18,10 @@ properties:
   reg:
     maxItems: 1
 
-  avdd-supply:
+  AVDD-supply:
     description: Analog power supply
 
-  dvdd-supply:
+  DVDD-supply:
     description: Digital power supply
 
   reset-gpios:

@@ -56,7 +56,7 @@ allOf:
       properties:
         dsd-path: false
 
-additionalProperties: false
+unevaluatedProperties: false
 
 examples:
   - |

Documentation/devicetree/bindings/sound/asahi-kasei,ak5558.yaml +2 -2

index d3d494ae8abfe..dc8f85f266bf3 100644
@@ -19,10 +19,10 @@ properties:
   reg:
     maxItems: 1
 
-  avdd-supply:
+  AVDD-supply:
     description: A 1.8V supply that powers up the AVDD pin.
 
-  dvdd-supply:
+  DVDD-supply:
     description: A 1.2V supply that powers up the DVDD pin.
 
   reset-gpios:

Documentation/hwmon/mpq8785.rst +15 -5

index bf8176b870868..b91fefb1a84cd 100644
@@ -5,6 +5,7 @@ Kernel driver mpq8785
 
 Supported chips:
 
+  * MPS MPM82504
   * MPS MPQ8785
 
     Prefix: 'mpq8785'

@@ -14,6 +15,14 @@ Author: Charles Hsu <[email protected]>
 Description
 -----------
 
+The MPM82504 is a quad 25A, scalable, fully integrated power module with a PMBus
+interface. The device offers a complete power solution that achieves up to 25A
+per output channel. The MPM82504 has four output channels that can be paralleled
+to provide 50A, 75A, or 100A of output current for flexible configurations.
+The device can also operate in parallel with the MPM3695-100 and additional
+MPM82504 devices to provide a higher output current. The MPM82504 operates
+at high efficiency across a wide load range.
+
 The MPQ8785 is a fully integrated, PMBus-compatible, high-frequency, synchronous
 buck converter. The MPQ8785 offers a very compact solution that achieves up to
 40A output current per phase, with excellent load and line regulation over a

@@ -23,18 +32,19 @@ output current load range.
 The PMBus interface provides converter configurations and key parameters
 monitoring.
 
-The MPQ8785 adopts MPS's proprietary multi-phase digital constant-on-time (MCOT)
+The devices adopts MPS's proprietary multi-phase digital constant-on-time (MCOT)
 control, which provides fast transient response and eases loop stabilization.
-The MCOT scheme also allows multiple MPQ8785 devices to be connected in parallel
-with excellent current sharing and phase interleaving for high-current
+The MCOT scheme also allows multiple devices or channels to be connected in
+parallel with excellent current sharing and phase interleaving for high-current
 applications.
 
 Fully integrated protection features include over-current protection (OCP),
 over-voltage protection (OVP), under-voltage protection (UVP), and
 over-temperature protection (OTP).
 
-The MPQ8785 requires a minimal number of readily available, standard external
-components, and is available in a TLGA (5mmx6mm) package.
+All supported modules require a minimal number of readily available, standard
+external components. The MPM82504 is available in a BGA (15mmx30mmx5.18mm)
+package and the MPQ8785 is available in a TLGA (5mmx6mm) package.
 
 Device compliant with:

Documentation/trace/events-pci.rst new file +74 -0

74 lines not on this page · raw message

Documentation/trace/index.rst +81 ~~-15~~

119 lines not on this page · raw message

Makefile +11 -2

index 94c1c8c7f899f..882a4dd080e67 100644
@@ -1,7 +1,7 @@
 # SPDX-License-Identifier: GPL-2.0
 VERSION = 6
 PATCHLEVEL = 12
-SUBLEVEL = 74
+SUBLEVEL = 75
 EXTRAVERSION =
 NAME = Baby Opossum Posse

@@ -1370,6 +1370,15 @@ ifneq ($(wildcard $(resolve_btfids_O)),)
 	$(Q)$(MAKE) -sC $(srctree)/tools/bpf/resolve_btfids O=$(resolve_btfids_O) clean
 endif
 
+PHONY += objtool_clean
+
+objtool_O = $(abspath $(objtree))/tools/objtool
+
+objtool_clean:
+ifneq ($(wildcard $(objtool_O)),)
+	$(Q)$(MAKE) -sC $(abs_srctree)/tools/objtool O=$(objtool_O) srctree=$(abs_srctree) clean
+endif
+
 tools/: FORCE
 	$(Q)mkdir -p $(objtree)/tools
 	$(Q)$(MAKE) O=$(abspath $(objtree)) subdir=tools -C $(srctree)/tools/

@@ -1527,7 +1536,7 @@ vmlinuxclean:
 	$(Q)$(CONFIG_SHELL) $(srctree)/scripts/link-vmlinux.sh clean
 	$(Q)$(if $(ARCH_POSTLINK), $(MAKE) -f $(ARCH_POSTLINK) clean)
 
-clean: archclean vmlinuxclean resolve_btfids_clean
+clean: archclean vmlinuxclean resolve_btfids_clean objtool_clean
 
 # mrproper - Delete all generated files, including .config
 #

arch/alpha/include/asm/pgtable.h +32 -1

index 02e8817a89212..8b620551304e9 100644
@@ -17,6 +17,7 @@
 #include <asm/processor.h>	/* For TASK_SIZE */
 #include <asm/machvec.h>
 #include <asm/setup.h>
+#include <linux/page_table_check.h>
 
 struct mm_struct;
 struct vm_area_struct;

@@ -213,6 +214,9 @@ extern inline void pud_set(pud_t * pudp, pmd_t * pmdp)
 { pud_val(*pudp) = _PAGE_TABLE | ((((unsigned long) pmdp) - PAGE_OFFSET) << (32-PAGE_SHIFT)); }
 
 
+extern void migrate_flush_tlb_page(struct vm_area_struct *vma,
+					unsigned long addr);
+
 extern inline unsigned long
 pmd_page_vaddr(pmd_t pmd)
 {

@@ -232,7 +236,7 @@ extern inline int pte_none(pte_t pte)		{ return !pte_val(pte); }
 extern inline int pte_present(pte_t pte)	{ return pte_val(pte) & _PAGE_VALID; }
 extern inline void pte_clear(struct mm_struct *mm, unsigned long addr, pte_t *ptep)
 {
-	pte_val(*ptep) = 0;
+	WRITE_ONCE(pte_val(*ptep), 0);
 }
 
 extern inline int pmd_none(pmd_t pmd)		{ return !pmd_val(pmd); }

@@ -294,6 +298,33 @@ extern inline pte_t * pte_offset_kernel(pmd_t * dir, unsigned long address)
 
 extern pgd_t swapper_pg_dir[1024];
 
+#ifdef CONFIG_COMPACTION
+#define __HAVE_ARCH_PTEP_GET_AND_CLEAR
+
+static inline pte_t ptep_get_and_clear(struct mm_struct *mm,
+					unsigned long address,
+					pte_t *ptep)
+{
+	pte_t pte = READ_ONCE(*ptep);
+
+	pte_clear(mm, address, ptep);
+	return pte;
+}
+
+#define __HAVE_ARCH_PTEP_CLEAR_FLUSH
+
+static inline pte_t ptep_clear_flush(struct vm_area_struct *vma,
+				unsigned long addr, pte_t *ptep)
+{
+	struct mm_struct *mm = vma->vm_mm;
+	pte_t pte = ptep_get_and_clear(mm, addr, ptep);
+
+	page_table_check_pte_clear(mm, pte);
+	migrate_flush_tlb_page(vma, addr);
+	return pte;
+}
+
+#endif
 /*
  * The Alpha doesn't have any external MMU info:  the kernel page
  * tables contain all the necessary information.

arch/alpha/include/asm/tlbflush.h +3 -1

index ba4b359d6c395..0c8529997f54e 100644
@@ -58,7 +58,9 @@ flush_tlb_other(struct mm_struct *mm)
 	unsigned long *mmc = &mm->context[smp_processor_id()];
 	/* Check it's not zero first to avoid cacheline ping pong
 	   when possible.  */
-	if (*mmc) *mmc = 0;
+
+	if (READ_ONCE(*mmc))
+		WRITE_ONCE(*mmc, 0);
 }
 
 #ifndef CONFIG_SMP

arch/alpha/mm/Makefile +1 -1

index 101dbd06b4ceb..2d05664058f64 100644
@@ -3,4 +3,4 @@
 # Makefile for the linux alpha-specific parts of the memory manager.
 #
 
-obj-y	:= init.o fault.o
+obj-y	:= init.o fault.o tlbflush.o

arch/alpha/mm/tlbflush.c new file +112 -0

112 lines not on this page · raw message

arch/arm/boot/dts/allwinner/sun5i-a13-utoo-p66.dts +1 -0

index be486d28d04fa..428cab5a0e906 100644
@@ -102,6 +102,7 @@ &touchscreen {
 	/* The P66 uses a different EINT then the reference design */
 	interrupts = <6 9 IRQ_TYPE_EDGE_FALLING>; /* EINT9 (PG9) */
 	/* The icn8318 binding expects wake-gpios instead of power-gpios */
+	/delete-property/ power-gpios;
 	wake-gpios = <&pio 1 3 GPIO_ACTIVE_HIGH>; /* PB3 */
 	touchscreen-size-x = <800>;
 	touchscreen-size-y = <480>;

arch/arm/boot/dts/nxp/lpc/lpc32xx.dtsi +2 -1

index 974410918f35b..7503074d2877c 100644
@@ -301,8 +301,9 @@ i2c2: i2c@400a8000 {
 			mpwm: mpwm@400e8000 {
 				compatible = "nxp,lpc3220-motor-pwm";
 				reg = <0x400e8000 0x78>;
+				clocks = <&clk LPC32XX_CLK_MCPWM>;
+				#pwm-cells = <3>;
 				status = "disabled";
-				#pwm-cells = <2>;
 			};
 		};

arch/arm/kernel/vdso.c +1 -0

index d499ad461b004..6e5494bf5a24d 100644
@@ -172,6 +172,7 @@ static void __init patch_vdso(void *ehdr)
 		vdso_nullpatch_one(&einfo, "__vdso_gettimeofday");
 		vdso_nullpatch_one(&einfo, "__vdso_clock_gettime");
 		vdso_nullpatch_one(&einfo, "__vdso_clock_gettime64");
+		vdso_nullpatch_one(&einfo, "__vdso_clock_getres");
 	}
 }

arch/arm/mach-omap2/control.c +10 -4

index 79860b23030de..eb6fc7c61b6e0 100644
@@ -732,7 +732,7 @@ int __init omap2_control_base_init(void)
  */
 int __init omap_control_init(void)
 {
-	struct device_node *np, *scm_conf;
+	struct device_node *np, *scm_conf, *clocks_node;
 	const struct of_device_id *match;
 	const struct omap_prcm_init_data *data;
 	int ret;

@@ -753,16 +753,19 @@ int __init omap_control_init(void)
 
 			if (IS_ERR(syscon)) {
 				ret = PTR_ERR(syscon);
-				goto of_node_put;
+				goto err_put_scm_conf;
 			}
 
-			if (of_get_child_by_name(scm_conf, "clocks")) {
+			clocks_node = of_get_child_by_name(scm_conf, "clocks");
+			if (clocks_node) {
+				of_node_put(clocks_node);
 				ret = omap2_clk_provider_init(scm_conf,
 							      data->index,
 							      syscon, NULL);
 				if (ret)
-					goto of_node_put;
+					goto err_put_scm_conf;
 			}
+			of_node_put(scm_conf);
 		} else {
 			/* No scm_conf found, direct access */
 			ret = omap2_clk_provider_init(np, data->index, NULL,

@@ -780,6 +783,9 @@ int __init omap_control_init(void)
 
 	return 0;
 
+err_put_scm_conf:
+	if (scm_conf)
+		of_node_put(scm_conf);
 of_node_put:
 	of_node_put(np);
 	return ret;

arch/arm/mm/physaddr.c +1 -1

index 3f263c840ebc4..1a37ebfacbba9 100644
@@ -38,7 +38,7 @@ static inline bool __virt_addr_valid(unsigned long x)
 phys_addr_t __virt_to_phys(unsigned long x)
 {
 	WARN(!__virt_addr_valid(x),
-	     "virt_to_phys used for non-linear address: %pK (%pS)\n",
+	     "virt_to_phys used for non-linear address: %px (%pS)\n",
 	     (void *)x, (void *)x);
 
 	return __virt_to_phys_nodebug(x);

arch/arm64/Kbuild +4 -0

index 5bfbf7d79c99b..d876bc0e54211 100644
@@ -1,4 +1,8 @@
 # SPDX-License-Identifier: GPL-2.0-only
+
+# Branch profiling isn't noinstr-safe
+subdir-ccflags-$(CONFIG_TRACE_BRANCH_PROFILING) += -DDISABLE_BRANCH_PROFILING
+
 obj-y			+= kernel/ mm/ net/
 obj-$(CONFIG_KVM)	+= kvm/
 obj-$(CONFIG_XEN)	+= xen/

arch/arm64/Kconfig +1 -0

index 40ae4dd961b15..0e2902f38e70e 100644
@@ -216,6 +216,7 @@ config ARM64
 	select HAVE_FTRACE_MCOUNT_RECORD
 	select HAVE_FUNCTION_TRACER
 	select HAVE_FUNCTION_ERROR_INJECTION
+	select HAVE_FUNCTION_GRAPH_FREGS
 	select HAVE_FUNCTION_GRAPH_TRACER
 	select HAVE_FUNCTION_GRAPH_RETVAL
 	select HAVE_GCC_PLUGINS

arch/arm64/boot/dts/amlogic/amlogic-c3.dtsi +7 -0

index d0cda759c25d0..edd92500ebc96 100644
@@ -570,6 +570,10 @@ sdio: mmc@88000 {
 				no-sd;
 				resets = <&reset RESET_SD_EMMC_A>;
 				status = "disabled";
+
+				assigned-clocks = <&clkc_periphs CLKID_SD_EMMC_A>;
+				assigned-clock-rates = <24000000>;
+
 			};
 
 			sd: mmc@8a000 {

@@ -585,6 +589,9 @@ sd: mmc@8a000 {
 				no-sdio;
 				resets = <&reset RESET_SD_EMMC_B>;
 				status = "disabled";
+
+				assigned-clocks = <&clkc_periphs CLKID_SD_EMMC_B>;
+				assigned-clock-rates = <24000000>;
 			};
 
 			nand: nand-controller@8d000 {

arch/arm64/boot/dts/amlogic/meson-axg.dtsi +6 -0

index e9b22868983db..4717c9666f2a5 100644
@@ -1923,6 +1923,9 @@ sd_emmc_b: mmc@5000 {
 					<&clkc CLKID_FCLK_DIV2>;
 				clock-names = "core", "clkin0", "clkin1";
 				resets = <&reset RESET_SD_EMMC_B>;
+
+				assigned-clocks = <&clkc CLKID_SD_EMMC_B_CLK0>;
+				assigned-clock-rates = <24000000>;
 			};
 
 			sd_emmc_c: mmc@7000 {

@@ -1935,6 +1938,9 @@ sd_emmc_c: mmc@7000 {
 					<&clkc CLKID_FCLK_DIV2>;
 				clock-names = "core", "clkin0", "clkin1";
 				resets = <&reset RESET_SD_EMMC_C>;
+
+				assigned-clocks = <&clkc CLKID_SD_EMMC_C_CLK0>;
+				assigned-clock-rates = <24000000>;
 			};
 
 			nfc: nand-controller@7800 {

arch/arm64/boot/dts/amlogic/meson-g12-common.dtsi +9 -0

index d08c97797010d..e0ddb28a34c29 100644
@@ -2408,6 +2408,9 @@ sd_emmc_a: mmc@ffe03000 {
 				 <&clkc CLKID_FCLK_DIV2>;
 			clock-names = "core", "clkin0", "clkin1";
 			resets = <&reset RESET_SD_EMMC_A>;
+
+			assigned-clocks = <&clkc CLKID_SD_EMMC_A_CLK0>;
+			assigned-clock-rates = <24000000>;
 		};
 
 		sd_emmc_b: mmc@ffe05000 {

@@ -2420,6 +2423,9 @@ sd_emmc_b: mmc@ffe05000 {
 				 <&clkc CLKID_FCLK_DIV2>;
 			clock-names = "core", "clkin0", "clkin1";
 			resets = <&reset RESET_SD_EMMC_B>;
+
+			assigned-clocks = <&clkc CLKID_SD_EMMC_B_CLK0>;
+			assigned-clock-rates = <24000000>;
 		};
 
 		sd_emmc_c: mmc@ffe07000 {

@@ -2432,6 +2438,9 @@ sd_emmc_c: mmc@ffe07000 {
 				 <&clkc CLKID_FCLK_DIV2>;
 			clock-names = "core", "clkin0", "clkin1";
 			resets = <&reset RESET_SD_EMMC_C>;
+
+			assigned-clocks = <&clkc CLKID_SD_EMMC_C_CLK0>;
+			assigned-clock-rates = <24000000>;
 		};
 
 		usb: usb@ffe09000 {

arch/arm64/boot/dts/amlogic/meson-gxbb.dtsi +9 -0

index ed00e67e6923a..851ae89dd17fa 100644
@@ -799,6 +799,9 @@ &sd_emmc_a {
 		 <&clkc CLKID_FCLK_DIV2>;
 	clock-names = "core", "clkin0", "clkin1";
 	resets = <&reset RESET_SD_EMMC_A>;
+
+	assigned-clocks = <&clkc CLKID_SD_EMMC_A_CLK0>;
+	assigned-clock-rates = <24000000>;
 };
 
 &sd_emmc_b {

@@ -807,6 +810,9 @@ &sd_emmc_b {
 		 <&clkc CLKID_FCLK_DIV2>;
 	clock-names = "core", "clkin0", "clkin1";
 	resets = <&reset RESET_SD_EMMC_B>;
+
+	assigned-clocks = <&clkc CLKID_SD_EMMC_B_CLK0>;
+	assigned-clock-rates = <24000000>;
 };
 
 &sd_emmc_c {

@@ -815,6 +821,9 @@ &sd_emmc_c {
 		 <&clkc CLKID_FCLK_DIV2>;
 	clock-names = "core", "clkin0", "clkin1";
 	resets = <&reset RESET_SD_EMMC_C>;
+
+	assigned-clocks = <&clkc CLKID_SD_EMMC_C_CLK0>;
+	assigned-clock-rates = <24000000>;
 };
 
 &simplefb_hdmi {

arch/arm64/boot/dts/amlogic/meson-gxl.dtsi +9 -0

index f58d1790de1cb..f7fafebafd809 100644
@@ -869,6 +869,9 @@ &sd_emmc_a {
 		 <&clkc CLKID_FCLK_DIV2>;
 	clock-names = "core", "clkin0", "clkin1";
 	resets = <&reset RESET_SD_EMMC_A>;
+
+	assigned-clocks = <&clkc CLKID_SD_EMMC_A_CLK0>;
+	assigned-clock-rates = <24000000>;
 };
 
 &sd_emmc_b {

@@ -877,6 +880,9 @@ &sd_emmc_b {
 		 <&clkc CLKID_FCLK_DIV2>;
 	clock-names = "core", "clkin0", "clkin1";
 	resets = <&reset RESET_SD_EMMC_B>;
+
+	assigned-clocks = <&clkc CLKID_SD_EMMC_B_CLK0>;
+	assigned-clock-rates = <24000000>;
 };
 
 &sd_emmc_c {

@@ -885,6 +891,9 @@ &sd_emmc_c {
 		 <&clkc CLKID_FCLK_DIV2>;
 	clock-names = "core", "clkin0", "clkin1";
 	resets = <&reset RESET_SD_EMMC_C>;
+
+	assigned-clocks = <&clkc CLKID_SD_EMMC_C_CLK0>;
+	assigned-clock-rates = <24000000>;
 };
 
 &simplefb_hdmi {

arch/arm64/boot/dts/amlogic/meson-s4.dtsi +11 -2

index 957577d986c06..7326aaa8d0ed7 100644
@@ -814,13 +814,16 @@ sdio: mmc@fe088000 {
 			reg = <0x0 0xfe088000 0x0 0x800>;
 			interrupts = <GIC_SPI 176 IRQ_TYPE_LEVEL_HIGH>;
 			clocks = <&clkc_periphs CLKID_SDEMMC_A>,
-				 <&xtal>,
+				 <&clkc_periphs CLKID_SD_EMMC_A>,
 				 <&clkc_pll CLKID_FCLK_DIV2>;
 			clock-names = "core", "clkin0", "clkin1";
 			resets = <&reset RESET_SD_EMMC_A>;
 			cap-sdio-irq;
 			keep-power-in-suspend;
 			status = "disabled";
+
+			assigned-clocks = <&clkc_periphs CLKID_SD_EMMC_A>;
+			assigned-clock-rates = <24000000>;
 		};
 
 		sd: mmc@fe08a000 {

@@ -833,6 +836,9 @@ sd: mmc@fe08a000 {
 			clock-names = "core", "clkin0", "clkin1";
 			resets = <&reset RESET_SD_EMMC_B>;
 			status = "disabled";
+
+			assigned-clocks = <&clkc_periphs CLKID_SD_EMMC_B>;
+			assigned-clock-rates = <24000000>;
 		};
 
 		emmc: mmc@fe08c000 {

@@ -840,13 +846,16 @@ emmc: mmc@fe08c000 {
 			reg = <0x0 0xfe08c000 0x0 0x800>;
 			interrupts = <GIC_SPI 178 IRQ_TYPE_EDGE_RISING>;
 			clocks = <&clkc_periphs CLKID_NAND>,
-				 <&xtal>,
+				 <&clkc_periphs CLKID_SD_EMMC_C>,
 				 <&clkc_pll CLKID_FCLK_DIV2>;
 			clock-names = "core", "clkin0", "clkin1";
 			resets = <&reset RESET_NAND_EMMC>;
 			no-sdio;
 			no-sd;
 			status = "disabled";
+
+			assigned-clocks = <&clkc_periphs CLKID_SD_EMMC_C>;
+			assigned-clock-rates = <24000000>;
 		};
 	};
 };

arch/arm64/boot/dts/apple/t8112-j473.dts +19 -0

index 06fe257f08be4..4ae1ce919dafc 100644
@@ -21,6 +21,25 @@ aliases {
 	};
 };
 
+/*
+ * Keep the power-domains used for the HDMI port on.
+ */
+&framebuffer0 {
+	power-domains = <&ps_dispext_cpu0>, <&ps_dptx_ext_phy>;
+};
+
+/*
+ * The M2 Mac mini uses dispext for the HDMI output so it's not necessary to
+ * keep disp0 power-domains always-on.
+ */
+&ps_disp0_sys {
+	/delete-property/ apple,always-on;
+};
+
+&ps_disp0_fe {
+	/delete-property/ apple,always-on;
+};
+
 /*
  * Force the bus number assignments so that we can declare some of the
  * on-board devices and properties that are populated by the bootloader

arch/arm64/boot/dts/freescale/imx8mp-tqma8mpql-mba8mp-ras314.dts +1 -1

index f7346b3d35fe5..a122f2ed5f531 100644
@@ -704,7 +704,7 @@ pinctrl_hdmi: hdmigrp {
 		fsl,pins = <MX8MP_IOMUXC_HDMI_DDC_SCL__HDMIMIX_HDMI_SCL	0x400001c2>,
 			   <MX8MP_IOMUXC_HDMI_DDC_SDA__HDMIMIX_HDMI_SDA	0x400001c2>,
 			   <MX8MP_IOMUXC_HDMI_HPD__HDMIMIX_HDMI_HPD	0x40000010>,
-			   <MX8MP_IOMUXC_HDMI_CEC__HDMIMIX_HDMI_CEC	0x40000154>;
+			   <MX8MP_IOMUXC_HDMI_CEC__HDMIMIX_HDMI_CEC	0x40000030>;
 	};
 
 	pinctrl_gpt1: gpt1grp {

arch/arm64/boot/dts/freescale/imx8mp-tqma8mpql-mba8mpxl.dts +1 -1

index e7c16a7ee6c26..773282002e6c6 100644
@@ -859,7 +859,7 @@ pinctrl_hdmi: hdmigrp {
 		fsl,pins = <MX8MP_IOMUXC_HDMI_DDC_SCL__HDMIMIX_HDMI_SCL	0x400001c2>,
 			   <MX8MP_IOMUXC_HDMI_DDC_SDA__HDMIMIX_HDMI_SDA	0x400001c2>,
 			   <MX8MP_IOMUXC_HDMI_HPD__HDMIMIX_HDMI_HPD	0x40000010>,
-			   <MX8MP_IOMUXC_HDMI_CEC__HDMIMIX_HDMI_CEC	0x40000010>;
+			   <MX8MP_IOMUXC_HDMI_CEC__HDMIMIX_HDMI_CEC	0x40000030>;
 	};
 
 	pinctrl_hoggpio2: hoggpio2grp {

arch/arm64/boot/dts/mediatek/mt8183-kukui-jacuzzi-pico6.dts +1 -1

index cce326aec1aa5..40af5656d6f15 100644
@@ -91,7 +91,7 @@ bluetooth@2 {
 
 &pio {
 	bt_pins_wakeup: bt-pins-wakeup {
-		piins-bt-wakeup {
+		pins-bt-wakeup {
 			pinmux = <PINMUX_GPIO42__FUNC_GPIO42>;
 			input-enable;
 		};

arch/arm64/boot/dts/nvidia/tegra210-smaug.dts +2 -0

index 2e5b6b2c1f56b..ff2952fae35c9 100644
@@ -1782,6 +1782,8 @@ usb2-0 {
 				status = "okay";
 				vbus-supply = <&usbc_vbus>;
 				mode = "otg";
+				usb-role-switch;
+				role-switch-default-mode = "host";
 			};
 
 			usb3-0 {

arch/arm64/boot/dts/qcom/msm8994-msft-lumia-octagon.dtsi +1 -1

index 10cd244dea4f7..ef8dfce8d9b2d 100644
@@ -378,7 +378,7 @@ &blsp2_i2c1 {
 	status = "okay";
 
 	sideinteraction: touch@2c {
-		compatible = "ad,ad7147_captouch";
+		compatible = "adi,ad7147_captouch";
 		reg = <0x2c>;
 
 		pinctrl-names = "default", "sleep";

arch/arm64/boot/dts/qcom/qcm2290.dtsi +6 -2

index e75e6354b2d52..dbc78b2d5095a 100644
@@ -1434,8 +1434,12 @@ usb_dwc3_ss: endpoint {
 
 		gpu: gpu@5900000 {
 			compatible = "qcom,adreno-07000200", "qcom,adreno";
-			reg = <0x0 0x05900000 0x0 0x40000>;
-			reg-names = "kgsl_3d0_reg_memory";
+			reg = <0x0 0x05900000 0x0 0x40000>,
+			      <0x0 0x0599e000 0x0 0x1000>,
+			      <0x0 0x05961000 0x0 0x800>;
+			reg-names = "kgsl_3d0_reg_memory",
+				    "cx_mem",
+				    "cx_dbgc";
 
 			interrupts = <GIC_SPI 177 IRQ_TYPE_LEVEL_HIGH>;

arch/arm64/boot/dts/qcom/qrb4210-rb2.dts +1 -1

index f99fb9159e0b6..547c6d4204601 100644
@@ -636,7 +636,7 @@ sdc2_card_det_n: sd-card-det-n-state {
 
 &uart3 {
 	interrupts-extended = <&intc GIC_SPI 330 IRQ_TYPE_LEVEL_HIGH>,
-			      <&tlmm 11 IRQ_TYPE_LEVEL_HIGH>;
+			      <&tlmm 11 IRQ_TYPE_EDGE_FALLING>;
 	pinctrl-0 = <&uart3_default>;
 	pinctrl-1 = <&uart3_sleep>;
 	pinctrl-names = "default", "sleep";

arch/arm64/boot/dts/qcom/sdm630.dtsi +2 -2

index c8da5cb8d04e9..37692d438d230 100644
@@ -591,8 +591,8 @@ qusb2_hstx_trim: hstx-trim@240 {
 			};
 
 			gpu_speed_bin: gpu-speed-bin@41a0 {
-				reg = <0x41a2 0x1>;
-				bits = <5 7>;
+				reg = <0x41a2 0x2>;
+				bits = <5 8>;
 			};
 		};

arch/arm64/boot/dts/qcom/sdm845-db845c.dts +7 -1

index 9a6d3d0c0ee43..8f3b31a30e247 100644
@@ -378,6 +378,12 @@ vreg_l21a_2p95: ldo21 {
 			regulator-initial-mode = <RPMH_REGULATOR_MODE_HPM>;
 		};
 
+		vreg_l23a_3p3: ldo23 {
+			regulator-min-microvolt = <3300000>;
+			regulator-max-microvolt = <3312000>;
+			regulator-initial-mode = <RPMH_REGULATOR_MODE_HPM>;
+		};
+
 		vreg_l24a_3p075: ldo24 {
 			regulator-min-microvolt = <3088000>;
 			regulator-max-microvolt = <3088000>;

@@ -858,7 +864,6 @@ &spi0 {
 	status = "okay";
 	pinctrl-names = "default";
 	pinctrl-0 = <&qup_spi0_default>;
-	cs-gpios = <&tlmm 3 GPIO_ACTIVE_LOW>;
 
 	can@0 {
 		compatible = "microchip,mcp2517fd";

@@ -1164,6 +1169,7 @@ &wifi {
 	vdd-1.8-xo-supply = <&vreg_l7a_1p8>;
 	vdd-1.3-rfa-supply = <&vreg_l17a_1p3>;
 	vdd-3.3-ch0-supply = <&vreg_l25a_3p3>;
+	vdd-3.3-ch1-supply = <&vreg_l23a_3p3>;
 
 	qcom,snoc-host-cap-8bit-quirk;
 	qcom,ath10k-calibration-variant = "Thundercomm_DB845C";

arch/arm64/boot/dts/qcom/sdm845-oneplus-common.dtsi +1 -1

index d0cbf9106a792..934bf9cfc5ac7 100644
@@ -156,7 +156,6 @@ ts_1p8_supply: ts-1p8-regulator {
 
 		gpio = <&tlmm 88 0>;
 		enable-active-high;
-		regulator-boot-on;
 	};
 };

@@ -247,6 +246,7 @@ vreg_l12a_1p8: ldo12 {
 			regulator-min-microvolt = <1800000>;
 			regulator-max-microvolt = <1800000>;
 			regulator-initial-mode = <RPMH_REGULATOR_MODE_HPM>;
+			regulator-boot-on;
 		};
 
 		vreg_l14a_1p88: ldo14 {

arch/arm64/boot/dts/qcom/sm6115.dtsi +6 -2

index 4adadfd1e51ae..e33da2975240f 100644
@@ -1688,8 +1688,12 @@ usb_dwc3_ss: endpoint {
 
 		gpu: gpu@5900000 {
 			compatible = "qcom,adreno-610.0", "qcom,adreno";
-			reg = <0x0 0x05900000 0x0 0x40000>;
-			reg-names = "kgsl_3d0_reg_memory";
+			reg = <0x0 0x05900000 0x0 0x40000>,
+			      <0x0 0x0599e000 0x0 0x1000>,
+			      <0x0 0x05961000 0x0 0x800>;
+			reg-names = "kgsl_3d0_reg_memory",
+				    "cx_mem",
+				    "cx_dbgc";
 
 			/* There's no (real) GMU, so we have to handle quite a bunch of clocks! */
 			clocks = <&gpucc GPU_CC_GX_GFX3D_CLK>,

arch/arm64/boot/dts/qcom/x1e80100.dtsi +12 -8

index 8536403e6ac99..6eef89ccdd121 100644
@@ -736,8 +736,8 @@ soc: soc@0 {
 
 		#address-cells = <2>;
 		#size-cells = <2>;
-		dma-ranges = <0 0 0 0 0x10 0>;
-		ranges = <0 0 0 0 0x10 0>;
+		dma-ranges = <0 0 0 0 0x100 0>;
+		ranges = <0 0 0 0 0x100 0>;
 
 		gcc: clock-controller@100000 {
 			compatible = "qcom,x1e80100-gcc";

@@ -2679,7 +2679,7 @@ usb_1_ss1_qmpphy: phy@fda000 {
 			reg = <0 0x00fda000 0 0x4000>;
 
 			clocks = <&gcc GCC_USB3_SEC_PHY_AUX_CLK>,
-				 <&rpmhcc RPMH_CXO_CLK>,
+				 <&tcsr TCSR_USB4_1_CLKREF_EN>,
 				 <&gcc GCC_USB3_SEC_PHY_COM_AUX_CLK>,
 				 <&gcc GCC_USB3_SEC_PHY_PIPE_CLK>;
 			clock-names = "aux",

@@ -2749,7 +2749,7 @@ usb_1_ss2_qmpphy: phy@fdf000 {
 			reg = <0 0x00fdf000 0 0x4000>;
 
 			clocks = <&gcc GCC_USB3_TERT_PHY_AUX_CLK>,
-				 <&rpmhcc RPMH_CXO_CLK>,
+				 <&tcsr TCSR_USB4_2_CLKREF_EN>,
 				 <&gcc GCC_USB3_TERT_PHY_COM_AUX_CLK>,
 				 <&gcc GCC_USB3_TERT_PHY_PIPE_CLK>;
 			clock-names = "aux",

@@ -5034,9 +5034,11 @@ mdss_dp2_phy: phy@aec2a00 {
 			      <0 0x0aec2000 0 0x1c8>;
 
 			clocks = <&dispcc DISP_CC_MDSS_DPTX2_AUX_CLK>,
-				 <&dispcc DISP_CC_MDSS_AHB_CLK>;
+				 <&dispcc DISP_CC_MDSS_AHB_CLK>,
+				 <&tcsr TCSR_EDP_CLKREF_EN>;
 			clock-names = "aux",
-				      "cfg_ahb";
+				      "cfg_ahb",
+				      "ref";
 
 			power-domains = <&rpmhpd RPMHPD_MX>;

@@ -5054,9 +5056,11 @@ mdss_dp3_phy: phy@aec5a00 {
 			      <0 0x0aec5000 0 0x1c8>;
 
 			clocks = <&dispcc DISP_CC_MDSS_DPTX3_AUX_CLK>,
-				 <&dispcc DISP_CC_MDSS_AHB_CLK>;
+				 <&dispcc DISP_CC_MDSS_AHB_CLK>,
+				 <&tcsr TCSR_EDP_CLKREF_EN>;
 			clock-names = "aux",
-				      "cfg_ahb";
+				      "cfg_ahb",
+				      "ref";
 
 			power-domains = <&rpmhpd RPMHPD_MX>;

arch/arm64/boot/dts/rockchip/rk3399-pinebook-pro.dts +0 -4

index a7afc83d2f266..20c5adb51d6d8 100644
@@ -428,10 +428,6 @@ &gpu {
 	status = "okay";
 };
 
-&hdmi_sound {
-	status = "okay";
-};
-
 &i2c0 {
 	clock-frequency = <400000>;
 	i2c-scl-falling-time-ns = <4>;

arch/arm64/boot/dts/ti/k3-j784s4-j742s2-main-common.dtsi +0 ~~-36~~

index 013c0d25d3481..079ccefeabe91 100644
@@ -2350,42 +2350,6 @@ watchdog3: watchdog@2230000 {
 		assigned-clock-parents = <&k3_clks 351 4>;
 	};
 
-	watchdog4: watchdog@2240000 {
-		compatible = "ti,j7-rti-wdt";
-		reg = <0x00 0x2240000 0x00 0x100>;
-		clocks = <&k3_clks 352 0>;
-		power-domains = <&k3_pds 352 TI_SCI_PD_EXCLUSIVE>;
-		assigned-clocks = <&k3_clks 352 0>;
-		assigned-clock-parents = <&k3_clks 352 4>;
-	};
-
-	watchdog5: watchdog@2250000 {
-		compatible = "ti,j7-rti-wdt";
-		reg = <0x00 0x2250000 0x00 0x100>;
-		clocks = <&k3_clks 353 0>;
-		power-domains = <&k3_pds 353 TI_SCI_PD_EXCLUSIVE>;
-		assigned-clocks = <&k3_clks 353 0>;
-		assigned-clock-parents = <&k3_clks 353 4>;
-	};
-
-	watchdog6: watchdog@2260000 {
-		compatible = "ti,j7-rti-wdt";
-		reg = <0x00 0x2260000 0x00 0x100>;
-		clocks = <&k3_clks 354 0>;
-		power-domains = <&k3_pds 354 TI_SCI_PD_EXCLUSIVE>;
-		assigned-clocks = <&k3_clks 354 0>;
-		assigned-clock-parents = <&k3_clks 354 4>;
-	};
-
-	watchdog7: watchdog@2270000 {
-		compatible = "ti,j7-rti-wdt";
-		reg = <0x00 0x2270000 0x00 0x100>;
-		clocks = <&k3_clks 355 0>;
-		power-domains = <&k3_pds 355 TI_SCI_PD_EXCLUSIVE>;
-		assigned-clocks = <&k3_clks 355 0>;
-		assigned-clock-parents = <&k3_clks 355 4>;
-	};
-
 	/*
 	 * The following RTI instances are coupled with MCU R5Fs, c7x and
 	 * GPU so keeping them reserved as these will be used by their

arch/arm64/boot/dts/ti/k3-j784s4-main.dtsi +47 ~~-11~~

70 lines not on this page · raw message

arch/arm64/boot/dts/xilinx/zynqmp.dtsi +0 -5

index e2ad5fb2cb0a4..0ff45540ca874 100644
@@ -187,11 +187,6 @@ psci {
 	};
 
 	firmware {
-		optee: optee  {
-			compatible = "linaro,optee-tz";
-			method = "smc";
-		};
-
 		zynqmp_firmware: zynqmp-firmware {
 			compatible = "xlnx,zynqmp-firmware";
 			#power-domain-cells = <1>;

arch/arm64/include/asm/ftrace.h +38 ~~-26~~

132 lines not on this page · raw message

arch/arm64/include/asm/pgtable.h +7 -2

index eb57ddb5ecc53..2de5a70a47ce3 100644
@@ -93,8 +93,6 @@ static inline pteval_t __phys_to_pte_val(phys_addr_t phys)
 	__pte(__phys_to_pte_val((phys_addr_t)(pfn) << PAGE_SHIFT) | pgprot_val(prot))
 
 #define pte_none(pte)		(!pte_val(pte))
-#define __pte_clear(mm, addr, ptep) \
-				__set_pte(ptep, __pte(0))
 #define pte_page(pte)		(pfn_to_page(pte_pfn(pte)))
 
 /*

@@ -1224,6 +1222,13 @@ static inline bool pud_user_accessible_page(pud_t pud)
 /*
  * Atomic pte/pmd modifications.
  */
+
+static inline void __pte_clear(struct mm_struct *mm,
+			       unsigned long addr, pte_t *ptep)
+{
+	__set_pte(ptep, __pte(0));
+}
+
 static inline int __ptep_test_and_clear_young(struct vm_area_struct *vma,
 					      unsigned long address,
 					      pte_t *ptep)

arch/arm64/include/asm/rwonce.h +1 -1

index 56f7b1d4d54b9..bd5fc880b9090 100644
@@ -62,7 +62,7 @@
 	default:							\
 		atomic = 0;						\
 	}								\
-	atomic ? (typeof(*__x))__u.__val : (*(volatile typeof(__x))__x);\
+	atomic ? (typeof(*__x))__u.__val : (*(volatile typeof(*__x) *)__x);\
 })
 
 #endif	/* !BUILD_VDSO */

arch/arm64/kernel/asm-offsets.c +11 ~~-23~~

index 020e01181a0f1..eccbe4d725f3b 100644
@@ -85,19 +85,19 @@ int main(void)
   DEFINE(PT_REGS_SIZE,		sizeof(struct pt_regs));
   BLANK();
 #ifdef CONFIG_DYNAMIC_FTRACE_WITH_ARGS
-  DEFINE(FREGS_X0,		offsetof(struct ftrace_regs, regs[0]));
-  DEFINE(FREGS_X2,		offsetof(struct ftrace_regs, regs[2]));
-  DEFINE(FREGS_X4,		offsetof(struct ftrace_regs, regs[4]));
-  DEFINE(FREGS_X6,		offsetof(struct ftrace_regs, regs[6]));
-  DEFINE(FREGS_X8,		offsetof(struct ftrace_regs, regs[8]));
-  DEFINE(FREGS_FP,		offsetof(struct ftrace_regs, fp));
-  DEFINE(FREGS_LR,		offsetof(struct ftrace_regs, lr));
-  DEFINE(FREGS_SP,		offsetof(struct ftrace_regs, sp));
-  DEFINE(FREGS_PC,		offsetof(struct ftrace_regs, pc));
+  DEFINE(FREGS_X0,		offsetof(struct __arch_ftrace_regs, regs[0]));
+  DEFINE(FREGS_X2,		offsetof(struct __arch_ftrace_regs, regs[2]));
+  DEFINE(FREGS_X4,		offsetof(struct __arch_ftrace_regs, regs[4]));
+  DEFINE(FREGS_X6,		offsetof(struct __arch_ftrace_regs, regs[6]));
+  DEFINE(FREGS_X8,		offsetof(struct __arch_ftrace_regs, regs[8]));
+  DEFINE(FREGS_FP,		offsetof(struct __arch_ftrace_regs, fp));
+  DEFINE(FREGS_LR,		offsetof(struct __arch_ftrace_regs, lr));
+  DEFINE(FREGS_SP,		offsetof(struct __arch_ftrace_regs, sp));
+  DEFINE(FREGS_PC,		offsetof(struct __arch_ftrace_regs, pc));
 #ifdef CONFIG_DYNAMIC_FTRACE_WITH_DIRECT_CALLS
-  DEFINE(FREGS_DIRECT_TRAMP,	offsetof(struct ftrace_regs, direct_tramp));
+  DEFINE(FREGS_DIRECT_TRAMP,	offsetof(struct __arch_ftrace_regs, direct_tramp));
 #endif
-  DEFINE(FREGS_SIZE,		sizeof(struct ftrace_regs));
+  DEFINE(FREGS_SIZE,		sizeof(struct __arch_ftrace_regs));
   BLANK();
 #endif
 #ifdef CONFIG_COMPAT

@@ -203,18 +203,6 @@ int main(void)
   DEFINE(FTRACE_OPS_FUNC,		offsetof(struct ftrace_ops, func));
 #endif
   BLANK();
-#ifdef CONFIG_FUNCTION_GRAPH_TRACER
-  DEFINE(FGRET_REGS_X0,			offsetof(struct fgraph_ret_regs, regs[0]));
-  DEFINE(FGRET_REGS_X1,			offsetof(struct fgraph_ret_regs, regs[1]));
-  DEFINE(FGRET_REGS_X2,			offsetof(struct fgraph_ret_regs, regs[2]));
-  DEFINE(FGRET_REGS_X3,			offsetof(struct fgraph_ret_regs, regs[3]));
-  DEFINE(FGRET_REGS_X4,			offsetof(struct fgraph_ret_regs, regs[4]));
-  DEFINE(FGRET_REGS_X5,			offsetof(struct fgraph_ret_regs, regs[5]));
-  DEFINE(FGRET_REGS_X6,			offsetof(struct fgraph_ret_regs, regs[6]));
-  DEFINE(FGRET_REGS_X7,			offsetof(struct fgraph_ret_regs, regs[7]));
-  DEFINE(FGRET_REGS_FP,			offsetof(struct fgraph_ret_regs, fp));
-  DEFINE(FGRET_REGS_SIZE,		sizeof(struct fgraph_ret_regs));
-#endif
 #ifdef CONFIG_DYNAMIC_FTRACE_WITH_DIRECT_CALLS
   DEFINE(FTRACE_OPS_DIRECT_CALL,	offsetof(struct ftrace_ops, direct_call));
 #endif

arch/arm64/kernel/entry-ftrace.S +18 ~~-14~~

index f0c16640ef215..169ccf600066b 100644
@@ -329,24 +329,28 @@ SYM_FUNC_END(ftrace_stub_graph)
  * @fp is checked against the value passed by ftrace_graph_caller().
  */
 SYM_CODE_START(return_to_handler)
-	/* save return value regs */
-	sub sp, sp, #FGRET_REGS_SIZE
-	stp x0, x1, [sp, #FGRET_REGS_X0]
-	stp x2, x3, [sp, #FGRET_REGS_X2]
-	stp x4, x5, [sp, #FGRET_REGS_X4]
-	stp x6, x7, [sp, #FGRET_REGS_X6]
-	str x29,    [sp, #FGRET_REGS_FP]	// parent's fp
+	/* Make room for ftrace_regs */
+	sub	sp, sp, #FREGS_SIZE
+
+	/* Save return value regs */
+	stp	x0, x1, [sp, #FREGS_X0]
+	stp	x2, x3, [sp, #FREGS_X2]
+	stp	x4, x5, [sp, #FREGS_X4]
+	stp	x6, x7, [sp, #FREGS_X6]
+
+	/* Save the callsite's FP */
+	str	x29, [sp, #FREGS_FP]
 
 	mov	x0, sp
-	bl	ftrace_return_to_handler	// addr = ftrace_return_to_hander(regs);
+	bl	ftrace_return_to_handler	// addr = ftrace_return_to_hander(fregs);
 	mov	x30, x0				// restore the original return address
 
-	/* restore return value regs */
-	ldp x0, x1, [sp, #FGRET_REGS_X0]
-	ldp x2, x3, [sp, #FGRET_REGS_X2]
-	ldp x4, x5, [sp, #FGRET_REGS_X4]
-	ldp x6, x7, [sp, #FGRET_REGS_X6]
-	add sp, sp, #FGRET_REGS_SIZE
+	/* Restore return value regs */
+	ldp	x0, x1, [sp, #FREGS_X0]
+	ldp	x2, x3, [sp, #FREGS_X2]
+	ldp	x4, x5, [sp, #FREGS_X4]
+	ldp	x6, x7, [sp, #FREGS_X6]
+	add	sp, sp, #FREGS_SIZE
 
 	ret
 SYM_CODE_END(return_to_handler)

arch/arm64/kernel/ftrace.c +5 -5

index b657f058bf4d5..06017bc1a555f 100644
@@ -23,10 +23,10 @@ struct fregs_offset {
 	int offset;
 };
 
-#define FREGS_OFFSET(n, field)				\
-{							\
-	.name = n,					\
-	.offset = offsetof(struct ftrace_regs, field),	\
+#define FREGS_OFFSET(n, field)					\
+{								\
+	.name = n,						\
+	.offset = offsetof(struct __arch_ftrace_regs, field),	\
 }
 
 static const struct fregs_offset fregs_offsets[] = {

@@ -488,7 +488,7 @@ void prepare_ftrace_return(unsigned long self_addr, unsigned long *parent,
 void ftrace_graph_func(unsigned long ip, unsigned long parent_ip,
 		       struct ftrace_ops *op, struct ftrace_regs *fregs)
 {
-	prepare_ftrace_return(ip, &fregs->lr, fregs->fp);
+	prepare_ftrace_return(ip, &arch_ftrace_regs(fregs)->lr, arch_ftrace_regs(fregs)->fp);
 }
 #else
 /*

arch/arm64/kernel/proton-pack.c +1 -0

index 31eaf15d2079a..ea8ca0714156b 100644
@@ -896,6 +896,7 @@ static u8 spectre_bhb_loop_affected(void)
 		MIDR_ALL_VERSIONS(MIDR_CORTEX_X2),
 		MIDR_ALL_VERSIONS(MIDR_NEOVERSE_N2),
 		MIDR_ALL_VERSIONS(MIDR_NEOVERSE_V1),
+		MIDR_ALL_VERSIONS(MIDR_HISI_TSV110),
 		{},
 	};
 	static const struct midr_range spectre_bhb_k24_list[] = {

arch/arm64/kernel/ptrace.c +3 -0

index 1a8f4284cb69a..ff1fe2d398692 100644
@@ -1454,6 +1454,9 @@ static int poe_get(struct task_struct *target,
 	if (!system_supports_poe())
 		return -EINVAL;
 
+	if (target == current)
+		current->thread.por_el0 = read_sysreg_s(SYS_POR_EL0);
+
 	return membuf_write(&to, &target->thread.por_el0,
 			    sizeof(target->thread.por_el0));
 }

arch/arm64/lib/delay.c +19 -4

index cb2062e7e2340..e278e060e78a9 100644
@@ -23,9 +23,24 @@ static inline unsigned long xloops_to_cycles(unsigned long xloops)
 	return (xloops * loops_per_jiffy * HZ) >> 32;
 }
 
+/*
+ * Force the use of CNTVCT_EL0 in order to have the same base as WFxT.
+ * This avoids some annoying issues when CNTVOFF_EL2 is not reset 0 on a
+ * KVM host running at EL1 until we do a vcpu_put() on the vcpu. When
+ * running at EL2, the effective offset is always 0.
+ *
+ * Note that userspace cannot change the offset behind our back either,
+ * as the vcpu mutex is held as long as KVM_RUN is in progress.
+ */
+static cycles_t notrace __delay_cycles(void)
+{
+	guard(preempt_notrace)();
+	return __arch_counter_get_cntvct_stable();
+}
+
 void __delay(unsigned long cycles)
 {
-	cycles_t start = get_cycles();
+	cycles_t start = __delay_cycles();
 
 	if (alternative_has_cap_unlikely(ARM64_HAS_WFXT)) {
 		u64 end = start + cycles;

@@ -35,17 +50,17 @@ void __delay(unsigned long cycles)
 		 * early, use a WFET loop to complete the delay.
 		 */
 		wfit(end);
-		while ((get_cycles() - start) < cycles)
+		while ((__delay_cycles() - start) < cycles)
 			wfet(end);
 	} else 	if (arch_timer_evtstrm_available()) {
 		const cycles_t timer_evt_period =
 			USECS_TO_CYCLES(ARCH_TIMER_EVT_STREAM_PERIOD_US);
 
-		while ((get_cycles() - start + timer_evt_period) < cycles)
+		while ((__delay_cycles() - start + timer_evt_period) < cycles)
 			wfe();
 	}
 
-	while ((get_cycles() - start) < cycles)
+	while ((__delay_cycles() - start) < cycles)
 		cpu_relax();
 }
 EXPORT_SYMBOL(__delay);

arch/loongarch/Kconfig +1 -1

index 5f35a8bd8996e..d402fcdf08610 100644
@@ -136,7 +136,7 @@ config LOONGARCH
 	select HAVE_FTRACE_MCOUNT_RECORD
 	select HAVE_FUNCTION_ARG_ACCESS_API
 	select HAVE_FUNCTION_ERROR_INJECTION
-	select HAVE_FUNCTION_GRAPH_RETVAL if HAVE_FUNCTION_GRAPH_TRACER
+	select HAVE_FUNCTION_GRAPH_FREGS
 	select HAVE_FUNCTION_GRAPH_TRACER
 	select HAVE_FUNCTION_TRACER
 	select HAVE_GCC_PLUGINS

arch/loongarch/include/asm/ftrace.h +7 ~~-46~~

79 lines not on this page · raw message

arch/loongarch/include/asm/topology.h +1 -1

index 50273c9187d02..23ff2718a0259 100644
@@ -12,7 +12,7 @@
 
 extern cpumask_t cpus_on_node[];
 
-#define cpumask_of_node(node)  (&cpus_on_node[node])
+#define cpumask_of_node(node)  ((node) == NUMA_NO_NODE ? cpu_all_mask : &cpus_on_node[node])
 
 struct pci_bus;
 extern int pcibus_to_node(struct pci_bus *);

arch/loongarch/kernel/asm-offsets.c +0 ~~-12~~

index d20d71d4bcae6..73954aa226646 100644
@@ -281,18 +281,6 @@ static void __used output_pbe_defines(void)
 }
 #endif
 
-#ifdef CONFIG_FUNCTION_GRAPH_TRACER
-static void __used output_fgraph_ret_regs_defines(void)
-{
-	COMMENT("LoongArch fgraph_ret_regs offsets.");
-	OFFSET(FGRET_REGS_A0, fgraph_ret_regs, regs[0]);
-	OFFSET(FGRET_REGS_A1, fgraph_ret_regs, regs[1]);
-	OFFSET(FGRET_REGS_FP, fgraph_ret_regs, fp);
-	DEFINE(FGRET_REGS_SIZE, sizeof(struct fgraph_ret_regs));
-	BLANK();
-}
-#endif
-
 static void __used output_kvm_defines(void)
 {
 	COMMENT("KVM/LoongArch Specific offsets.");

arch/loongarch/kernel/ftrace_dyn.c +1 -1

index bff058317062e..18056229e22e4 100644
@@ -241,7 +241,7 @@ void prepare_ftrace_return(unsigned long self_addr, unsigned long *parent)
 void ftrace_graph_func(unsigned long ip, unsigned long parent_ip,
 		       struct ftrace_ops *op, struct ftrace_regs *fregs)
 {
-	struct pt_regs *regs = &fregs->regs;
+	struct pt_regs *regs = &arch_ftrace_regs(fregs)->regs;
 	unsigned long *parent = (unsigned long *)&regs->regs[1];
 
 	prepare_ftrace_return(ip, (unsigned long *)parent);

arch/loongarch/kernel/mcount.S +10 -7

index 3015896016a0b..b6850503e061b 100644
@@ -79,10 +79,11 @@ SYM_FUNC_START(ftrace_graph_caller)
 SYM_FUNC_END(ftrace_graph_caller)
 
 SYM_FUNC_START(return_to_handler)
-	PTR_ADDI	sp, sp, -FGRET_REGS_SIZE
-	PTR_S		a0, sp, FGRET_REGS_A0
-	PTR_S		a1, sp, FGRET_REGS_A1
-	PTR_S		zero, sp, FGRET_REGS_FP
+	/* Save return value regs */
+	PTR_ADDI	sp, sp, -PT_SIZE
+	PTR_S		a0, sp, PT_R4
+	PTR_S		a1, sp, PT_R5
+	PTR_S		zero, sp, PT_R22
 
 	move		a0, sp
 	bl		ftrace_return_to_handler

@@ -90,9 +91,11 @@ SYM_FUNC_START(return_to_handler)
 	/* Restore the real parent address: a0 -> ra */
 	move		ra, a0
 
-	PTR_L		a0, sp, FGRET_REGS_A0
-	PTR_L		a1, sp, FGRET_REGS_A1
-	PTR_ADDI	sp, sp, FGRET_REGS_SIZE
+	/* Restore return value regs */
+	PTR_L		a0, sp, PT_R4
+	PTR_L		a1, sp, PT_R5
+	PTR_ADDI	sp, sp, PT_SIZE
+
 	jr		ra
 SYM_FUNC_END(return_to_handler)
 #endif /* CONFIG_FUNCTION_GRAPH_TRACER */

arch/loongarch/kernel/mcount_dyn.S +7 -7

index 4e05adb405043..5729c20e5b8b0 100644
@@ -144,19 +144,19 @@ SYM_CODE_END(ftrace_graph_caller)
 SYM_CODE_START(return_to_handler)
 	UNWIND_HINT_UNDEFINED
 	/* Save return value regs */
-	PTR_ADDI	sp, sp, -FGRET_REGS_SIZE
-	PTR_S		a0, sp, FGRET_REGS_A0
-	PTR_S		a1, sp, FGRET_REGS_A1
-	PTR_S		zero, sp, FGRET_REGS_FP
+	PTR_ADDI	sp, sp, -PT_SIZE
+	PTR_S		a0, sp, PT_R4
+	PTR_S		a1, sp, PT_R5
+	PTR_S		zero, sp, PT_R22
 
 	move		a0, sp
 	bl		ftrace_return_to_handler
 	move		ra, a0
 
 	/* Restore return value regs */
-	PTR_L		a0, sp, FGRET_REGS_A0
-	PTR_L		a1, sp, FGRET_REGS_A1
-	PTR_ADDI	sp, sp, FGRET_REGS_SIZE
+	PTR_L		a0, sp, PT_R4
+	PTR_L		a1, sp, PT_R5
+	PTR_ADDI	sp, sp, PT_SIZE
 
 	jr		ra
 SYM_CODE_END(return_to_handler)

arch/loongarch/kernel/setup.c +1 -0

index 3cfe591b66a4c..2c2586b6e08ce 100644
@@ -421,6 +421,7 @@ static void __init arch_mem_init(char **cmdline_p)
 				   PFN_UP(__pa_symbol(&__nosave_end)));
 
 	memblock_dump_all();
+	memblock_set_bottom_up(false);
 
 	early_memtest(PFN_PHYS(ARCH_PFN_OFFSET), PFN_PHYS(max_low_pfn));
 }

arch/loongarch/kernel/unwind_orc.c +1 -1

index b4b4ac8dbf417..471652c0c8653 100644
@@ -507,7 +507,7 @@ bool unwind_next_frame(struct unwind_state *state)
 
 	state->pc = bt_address(pc);
 	if (!state->pc) {
-		pr_err("cannot find unwind pc at %p\n", (void *)pc);
+		pr_err("cannot find unwind pc at %px\n", (void *)pc);
 		goto err;
 	}

arch/loongarch/kernel/unwind_prologue.c +1 -1

index 929ae240280a5..c9ee6892d81c7 100644
@@ -64,7 +64,7 @@ static inline bool scan_handlers(unsigned long entry_offset)
 
 static inline bool fix_exception(unsigned long pc)
 {
-#ifdef CONFIG_NUMA
+#if defined(CONFIG_NUMA) && !defined(CONFIG_PREEMPT_RT)
 	int cpu;
 
 	for_each_possible_cpu(cpu) {

arch/loongarch/mm/tlb.c +1 -1

index 3b427b319db21..f46c15d6e7eae 100644
@@ -202,7 +202,7 @@ void __update_tlb(struct vm_area_struct *vma, unsigned long address, pte_t *ptep
 	local_irq_restore(flags);
 }
 
-static void setup_ptwalker(void)
+static void __no_sanitize_address setup_ptwalker(void)
 {
 	unsigned long pwctl0, pwctl1;
 	unsigned long pgd_i = 0, pgd_w = 0;

arch/m68k/lib/memmove.c +18 -0

index 6519f7f349f66..e33f00b02e4c0 100644
@@ -24,6 +24,15 @@ void *memmove(void *dest, const void *src, size_t n)
 			src = csrc;
 			n--;
 		}
+#if defined(CONFIG_M68000)
+		if ((long)src & 1) {
+			char *cdest = dest;
+			const char *csrc = src;
+			for (; n; n--)
+				*cdest++ = *csrc++;
+			return xdest;
+		}
+#endif
 		if (n > 2 && (long)dest & 2) {
 			short *sdest = dest;
 			const short *ssrc = src;

@@ -66,6 +75,15 @@ void *memmove(void *dest, const void *src, size_t n)
 			src = csrc;
 			n--;
 		}
+#if defined(CONFIG_M68000)
+		if ((long)src & 1) {
+			char *cdest = dest;
+			const char *csrc = src;
+			for (; n; n--)
+				*--cdest = *--csrc;
+			return xdest;
+		}
+#endif
 		if (n > 2 && (long)dest & 2) {
 			short *sdest = dest;
 			const short *ssrc = src;

arch/mips/include/asm/mach-loongson64/topology.h +1 -1

index 3414a1fd17835..89bb4deab98a6 100644
@@ -7,7 +7,7 @@
 #define cpu_to_node(cpu)	(cpu_logical_map(cpu) >> 2)
 
 extern cpumask_t __node_cpumask[];
-#define cpumask_of_node(node)	(&__node_cpumask[node])
+#define cpumask_of_node(node)	  ((node) == NUMA_NO_NODE ? cpu_all_mask : &__node_cpumask[node])
 
 struct pci_bus;
 extern int pcibus_to_node(struct pci_bus *);

arch/mips/kernel/relocate.c +13 -0

index cda7983e7c18d..ba3b82f0341a9 100644
@@ -420,7 +420,20 @@ void *__init relocate_kernel(void)
 			goto out;
 
 		/* The current thread is now within the relocated image */
+#ifndef CONFIG_CC_IS_CLANG
 		__current_thread_info = RELOCATED(&init_thread_union);
+#else
+		/*
+		 * LLVM may wrongly restore $gp ($28) in epilog even if it's
+		 * intentionally modified. Work around this by using inline
+		 * assembly to assign $gp. $gp couldn't be listed as output or
+		 * clobber, or LLVM will still restore its original value.
+		 * See also LLVM upstream issue
+		 * https://github.com/llvm/llvm-project/issues/176546
+		 */
+		asm volatile("move $28, %0" : :
+			     "r" (RELOCATED(&init_thread_union)));
+#endif
 
 		/* Return the new kernel's entry point */
 		kernel_entry = RELOCATED(start_kernel);

arch/mips/rb532/devices.c +3 -2

index b7f6f782d9a13..ffa4d38ca95df 100644
@@ -212,11 +212,12 @@ static struct platform_device rb532_wdt = {
 static struct plat_serial8250_port rb532_uart_res[] = {
 	{
 		.type           = PORT_16550A,
-		.membase	= (char *)KSEG1ADDR(REGBASE + UART0BASE),
+		.mapbase        = REGBASE + UART0BASE,
+		.mapsize        = 0x1000,
 		.irq		= UART0_IRQ,
 		.regshift	= 2,
 		.iotype		= UPIO_MEM,
-		.flags		= UPF_BOOT_AUTOCONF,
+		.flags		= UPF_BOOT_AUTOCONF | UPF_IOREMAP,
 	},
 	{
 		.flags		= 0,

arch/openrisc/include/asm/barrier.h +2 -0

index 7538294721bed..8e592c9909023 100644
@@ -4,6 +4,8 @@
 
 #define mb() asm volatile ("l.msync" ::: "memory")
 
+#define nop() asm volatile ("l.nop")
+
 #include <asm-generic/barrier.h>
 
 #endif /* __ASM_BARRIER_H */

arch/parisc/kernel/drivers.c +1 -1

index 1e793f770f719..5dd7f862db2bd 100644
@@ -435,7 +435,7 @@ static struct parisc_device * __init create_tree_node(char id,
 	dev->dev.dma_mask = &dev->dma_mask;
 	dev->dev.coherent_dma_mask = dev->dma_mask;
 	if (device_register(&dev->dev)) {
-		kfree(dev);
+		put_device(&dev->dev);
 		return NULL;
 	}

arch/parisc/kernel/process.c +3 -0

index ed93bd8c15453..d7b0f233f2cc9 100644
@@ -85,6 +85,9 @@ void machine_restart(char *cmd)
 #endif
 	/* set up a new led state on systems shipped with a LED State panel */
 	pdc_chassis_send_status(PDC_CHASSIS_DIRECT_SHUTDOWN);
+
+	/* prevent interrupts during reboot */
+	set_eiem(0);
 	
 	/* "Normal" system reset */
 	pdc_do_reset();

arch/powerpc/include/asm/eeh.h +2 -0

index 5e34611de9ef4..b7ebb4ac2c710 100644
@@ -289,6 +289,8 @@ void eeh_pe_dev_traverse(struct eeh_pe *root,
 void eeh_pe_restore_bars(struct eeh_pe *pe);
 const char *eeh_pe_loc_get(struct eeh_pe *pe);
 struct pci_bus *eeh_pe_bus_get(struct eeh_pe *pe);
+const char *eeh_pe_loc_get_bus(struct pci_bus *bus);
+struct pci_bus *eeh_pe_bus_get_nolock(struct eeh_pe *pe);
 
 void eeh_show_enabled(void);
 int __init eeh_init(struct eeh_ops *ops);

arch/powerpc/include/asm/ftrace.h +10 ~~-24~~

index 559560286e6d0..407ce6eccc04f 100644
@@ -32,42 +32,28 @@ struct dyn_arch_ftrace {
 int ftrace_init_nop(struct module *mod, struct dyn_ftrace *rec);
 #define ftrace_init_nop ftrace_init_nop
 
-struct ftrace_regs {
-	struct pt_regs regs;
-};
+#include <linux/ftrace_regs.h>
 
 static __always_inline struct pt_regs *arch_ftrace_get_regs(struct ftrace_regs *fregs)
 {
 	/* We clear regs.msr in ftrace_call */
-	return fregs->regs.msr ? &fregs->regs : NULL;
+	return arch_ftrace_regs(fregs)->regs.msr ? &arch_ftrace_regs(fregs)->regs : NULL;
 }
 
+#define arch_ftrace_fill_perf_regs(fregs, _regs) do {		\
+		(_regs)->result = 0;				\
+		(_regs)->nip = arch_ftrace_regs(fregs)->regs.nip;		\
+		(_regs)->gpr[1] = arch_ftrace_regs(fregs)->regs.gpr[1];		\
+		asm volatile("mfmsr %0" : "=r" ((_regs)->msr));	\
+	} while (0)
+
 static __always_inline void
 ftrace_regs_set_instruction_pointer(struct ftrace_regs *fregs,
 				    unsigned long ip)
 {
-	regs_set_return_ip(&fregs->regs, ip);
-}
-
-static __always_inline unsigned long
-ftrace_regs_get_instruction_pointer(struct ftrace_regs *fregs)
-{
-	return instruction_pointer(&fregs->regs);
+	regs_set_return_ip(&arch_ftrace_regs(fregs)->regs, ip);
 }
 
-#define ftrace_regs_get_argument(fregs, n) \
-	regs_get_kernel_argument(&(fregs)->regs, n)
-#define ftrace_regs_get_stack_pointer(fregs) \
-	kernel_stack_pointer(&(fregs)->regs)
-#define ftrace_regs_return_value(fregs) \
-	regs_return_value(&(fregs)->regs)
-#define ftrace_regs_set_return_value(fregs, ret) \
-	regs_set_return_value(&(fregs)->regs, ret)
-#define ftrace_override_function_with_return(fregs) \
-	override_function_with_return(&(fregs)->regs)
-#define ftrace_regs_query_register_offset(name) \
-	regs_query_register_offset(name)
-
 struct ftrace_ops;
 
 #define ftrace_graph_func ftrace_graph_func

arch/powerpc/include/asm/kup.h +0 -2

index 2bb03d941e3e8..6737416dde9f0 100644
@@ -134,7 +134,6 @@ static __always_inline void kuap_assert_locked(void)
 
 static __always_inline void allow_read_from_user(const void __user *from, unsigned long size)
 {
-	barrier_nospec();
 	allow_user_access(NULL, from, size, KUAP_READ);
 }

@@ -146,7 +145,6 @@ static __always_inline void allow_write_to_user(void __user *to, unsigned long s
 static __always_inline void allow_read_write_user(void __user *to, const void __user *from,
 						  unsigned long size)
 {
-	barrier_nospec();
 	allow_user_access(to, from, size, KUAP_READ_WRITE);
 }

arch/powerpc/include/asm/uaccess.h +4 -0

index 4f5a46a77fa2b..3987a5c33558b 100644
@@ -301,6 +301,7 @@ do {								\
 	__typeof__(sizeof(*(ptr))) __gu_size = sizeof(*(ptr));	\
 								\
 	might_fault();					\
+	barrier_nospec();					\
 	allow_read_from_user(__gu_addr, __gu_size);		\
 	__get_user_size_allowed(__gu_val, __gu_addr, __gu_size, __gu_err);	\
 	prevent_read_from_user(__gu_addr, __gu_size);		\

@@ -329,6 +330,7 @@ raw_copy_in_user(void __user *to, const void __user *from, unsigned long n)
 {
 	unsigned long ret;
 
+	barrier_nospec();
 	allow_read_write_user(to, from, n);
 	ret = __copy_tofrom_user(to, from, n);
 	prevent_read_write_user(to, from, n);

@@ -415,6 +417,7 @@ static __must_check __always_inline bool user_access_begin(const void __user *pt
 
 	might_fault();
 
+	barrier_nospec();
 	allow_read_write_user((void __user *)ptr, ptr, len);
 	return true;
 }

@@ -431,6 +434,7 @@ user_read_access_begin(const void __user *ptr, size_t len)
 
 	might_fault();
 
+	barrier_nospec();
 	allow_read_from_user(ptr, len);
 	return true;
 }

arch/powerpc/kernel/eeh_driver.c +6 -5

index c73e4225e84a5..51a6d881c2292 100644
@@ -846,7 +846,7 @@ void eeh_handle_normal_event(struct eeh_pe *pe)
 
 	pci_lock_rescan_remove();
 
-	bus = eeh_pe_bus_get(pe);
+	bus = eeh_pe_bus_get_nolock(pe);
 	if (!bus) {
 		pr_err("%s: Cannot find PCI bus for PHB#%x-PE#%x\n",
 			__func__, pe->phb->global_number, pe->addr);

@@ -886,14 +886,15 @@ void eeh_handle_normal_event(struct eeh_pe *pe)
 	/* Log the event */
 	if (pe->type & EEH_PE_PHB) {
 		pr_err("EEH: Recovering PHB#%x, location: %s\n",
-			pe->phb->global_number, eeh_pe_loc_get(pe));
+			pe->phb->global_number, eeh_pe_loc_get_bus(bus));
 	} else {
 		struct eeh_pe *phb_pe = eeh_phb_pe_get(pe->phb);
 
 		pr_err("EEH: Recovering PHB#%x-PE#%x\n",
 		       pe->phb->global_number, pe->addr);
 		pr_err("EEH: PE location: %s, PHB location: %s\n",
-		       eeh_pe_loc_get(pe), eeh_pe_loc_get(phb_pe));
+		       eeh_pe_loc_get_bus(bus),
+		       eeh_pe_loc_get_bus(eeh_pe_bus_get_nolock(phb_pe)));
 	}
 
 #ifdef CONFIG_STACKTRACE

@@ -1098,7 +1099,7 @@ void eeh_handle_normal_event(struct eeh_pe *pe)
 		eeh_pe_state_clear(pe, EEH_PE_PRI_BUS, true);
 		eeh_pe_dev_mode_mark(pe, EEH_DEV_REMOVED);
 
-		bus = eeh_pe_bus_get(pe);
+		bus = eeh_pe_bus_get_nolock(pe);
 		if (bus)
 			pci_hp_remove_devices(bus);
 		else

@@ -1222,7 +1223,7 @@ void eeh_handle_special_event(void)
 				    (phb_pe->state & EEH_PE_RECOVERING))
 					continue;
 
-				bus = eeh_pe_bus_get(phb_pe);
+				bus = eeh_pe_bus_get_nolock(phb_pe);
 				if (!bus) {
 					pr_err("%s: Cannot find PCI bus for "
 					       "PHB#%x-PE#%x\n",

arch/powerpc/kernel/eeh_pe.c +70 -4

102 lines not on this page · raw message

arch/powerpc/kernel/smp.c +2 -0

index 4ab9b8cee77a1..09b2ccf387118 100644
@@ -821,6 +821,8 @@ static int parse_thread_groups(struct device_node *dn,
 
 	count = of_property_count_u32_elems(dn, "ibm,thread-groups");
 	thread_group_array = kcalloc(count, sizeof(u32), GFP_KERNEL);
+	if (!thread_group_array)
+		return -ENOMEM;
 	ret = of_property_read_u32_array(dn, "ibm,thread-groups",
 					 thread_group_array, count);
 	if (ret)

arch/powerpc/kernel/trace/ftrace.c +2 -2

index d8d6b4fd9a14c..df41f4a7c738b 100644
@@ -421,7 +421,7 @@ int __init ftrace_dyn_arch_init(void)
 void ftrace_graph_func(unsigned long ip, unsigned long parent_ip,
 		       struct ftrace_ops *op, struct ftrace_regs *fregs)
 {
-	unsigned long sp = fregs->regs.gpr[1];
+	unsigned long sp = arch_ftrace_regs(fregs)->regs.gpr[1];
 	int bit;
 
 	if (unlikely(ftrace_graph_is_dead()))

@@ -439,6 +439,6 @@ void ftrace_graph_func(unsigned long ip, unsigned long parent_ip,
 
 	ftrace_test_recursion_unlock(bit);
 out:
-	fregs->regs.link = parent_ip;
+	arch_ftrace_regs(fregs)->regs.link = parent_ip;
 }
 #endif /* CONFIG_FUNCTION_GRAPH_TRACER */

arch/powerpc/kernel/trace/ftrace_64_pg.c +1 -1

index 12fab1803bcf4..d3c5552e4984d 100644
@@ -829,7 +829,7 @@ __prepare_ftrace_return(unsigned long parent, unsigned long ip, unsigned long sp
 void ftrace_graph_func(unsigned long ip, unsigned long parent_ip,
 		       struct ftrace_ops *op, struct ftrace_regs *fregs)
 {
-	fregs->regs.link = __prepare_ftrace_return(parent_ip, ip, fregs->regs.gpr[1]);
+	arch_ftrace_regs(fregs)->regs.link = __prepare_ftrace_return(parent_ip, ip, arch_ftrace_regs(fregs)->regs.gpr[1]);
 }
 #else
 unsigned long prepare_ftrace_return(unsigned long parent, unsigned long ip,

arch/riscv/Kconfig +1 -1

index d160c3b830266..9e8667a523d55 100644
@@ -144,7 +144,7 @@ config RISCV
 	select HAVE_DYNAMIC_FTRACE_WITH_ARGS if HAVE_DYNAMIC_FTRACE
 	select HAVE_FTRACE_MCOUNT_RECORD if !XIP_KERNEL
 	select HAVE_FUNCTION_GRAPH_TRACER
-	select HAVE_FUNCTION_GRAPH_RETVAL if HAVE_FUNCTION_GRAPH_TRACER
+	select HAVE_FUNCTION_GRAPH_FREGS
 	select HAVE_FUNCTION_TRACER if !XIP_KERNEL && !PREEMPTION
 	select HAVE_EBPF_JIT if MMU
 	select HAVE_GUP_FAST if MMU

arch/riscv/include/asm/ftrace.h +32 ~~-30~~

114 lines not on this page · raw message

arch/riscv/kernel/asm-offsets.c +14 ~~-14~~

index 05c6152a65310..dfed9986b45ed 100644
@@ -497,19 +497,19 @@ void asm_offsets(void)
 	OFFSET(STACKFRAME_RA, stackframe, ra);
 
 #ifdef CONFIG_DYNAMIC_FTRACE_WITH_ARGS
-	DEFINE(FREGS_SIZE_ON_STACK, ALIGN(sizeof(struct ftrace_regs), STACK_ALIGN));
-	DEFINE(FREGS_EPC,	    offsetof(struct ftrace_regs, epc));
-	DEFINE(FREGS_RA,	    offsetof(struct ftrace_regs, ra));
-	DEFINE(FREGS_SP,	    offsetof(struct ftrace_regs, sp));
-	DEFINE(FREGS_S0,	    offsetof(struct ftrace_regs, s0));
-	DEFINE(FREGS_T1,	    offsetof(struct ftrace_regs, t1));
-	DEFINE(FREGS_A0,	    offsetof(struct ftrace_regs, a0));
-	DEFINE(FREGS_A1,	    offsetof(struct ftrace_regs, a1));
-	DEFINE(FREGS_A2,	    offsetof(struct ftrace_regs, a2));
-	DEFINE(FREGS_A3,	    offsetof(struct ftrace_regs, a3));
-	DEFINE(FREGS_A4,	    offsetof(struct ftrace_regs, a4));
-	DEFINE(FREGS_A5,	    offsetof(struct ftrace_regs, a5));
-	DEFINE(FREGS_A6,	    offsetof(struct ftrace_regs, a6));
-	DEFINE(FREGS_A7,	    offsetof(struct ftrace_regs, a7));
+	DEFINE(FREGS_SIZE_ON_STACK, ALIGN(sizeof(struct __arch_ftrace_regs), STACK_ALIGN));
+	DEFINE(FREGS_EPC,	    offsetof(struct __arch_ftrace_regs, epc));
+	DEFINE(FREGS_RA,	    offsetof(struct __arch_ftrace_regs, ra));
+	DEFINE(FREGS_SP,	    offsetof(struct __arch_ftrace_regs, sp));
+	DEFINE(FREGS_S0,	    offsetof(struct __arch_ftrace_regs, s0));
+	DEFINE(FREGS_T1,	    offsetof(struct __arch_ftrace_regs, t1));
+	DEFINE(FREGS_A0,	    offsetof(struct __arch_ftrace_regs, a0));
+	DEFINE(FREGS_A1,	    offsetof(struct __arch_ftrace_regs, a1));
+	DEFINE(FREGS_A2,	    offsetof(struct __arch_ftrace_regs, a2));
+	DEFINE(FREGS_A3,	    offsetof(struct __arch_ftrace_regs, a3));
+	DEFINE(FREGS_A4,	    offsetof(struct __arch_ftrace_regs, a4));
+	DEFINE(FREGS_A5,	    offsetof(struct __arch_ftrace_regs, a5));
+	DEFINE(FREGS_A6,	    offsetof(struct __arch_ftrace_regs, a6));
+	DEFINE(FREGS_A7,	    offsetof(struct __arch_ftrace_regs, a7));
 #endif
 }

arch/riscv/kernel/ftrace.c +1 -1

index 4b95c574fd045..5081ad886841f 100644
@@ -214,7 +214,7 @@ void prepare_ftrace_return(unsigned long *parent, unsigned long self_addr,
 void ftrace_graph_func(unsigned long ip, unsigned long parent_ip,
 		       struct ftrace_ops *op, struct ftrace_regs *fregs)
 {
-	prepare_ftrace_return(&fregs->ra, ip, fregs->s0);
+	prepare_ftrace_return(&arch_ftrace_regs(fregs)->ra, ip, arch_ftrace_regs(fregs)->s0);
 }
 #else /* CONFIG_DYNAMIC_FTRACE_WITH_ARGS */
 extern void ftrace_graph_call(void);

arch/riscv/kernel/mcount.S +13 ~~-11~~

index 3a42f6287909d..068168046e0ef 100644
@@ -12,6 +12,8 @@
 #include <asm/asm-offsets.h>
 #include <asm/ftrace.h>
 
+#define ABI_SIZE_ON_STACK	80
+
 	.text
 
 	.macro SAVE_ABI_STATE

@@ -26,12 +28,12 @@
 	 * register if a0 was not saved.
 	 */
 	.macro SAVE_RET_ABI_STATE
-	addi	sp, sp, -4*SZREG
-	REG_S	s0, 2*SZREG(sp)
-	REG_S	ra, 3*SZREG(sp)
-	REG_S	a0, 1*SZREG(sp)
-	REG_S	a1, 0*SZREG(sp)
-	addi	s0, sp, 4*SZREG
+	addi	sp, sp, -ABI_SIZE_ON_STACK
+	REG_S	ra, 1*SZREG(sp)
+	REG_S	s0, 8*SZREG(sp)
+	REG_S	a0, 10*SZREG(sp)
+	REG_S	a1, 11*SZREG(sp)
+	addi	s0, sp, ABI_SIZE_ON_STACK
 	.endm
 
 	.macro RESTORE_ABI_STATE

@@ -41,11 +43,11 @@
 	.endm
 
 	.macro RESTORE_RET_ABI_STATE
-	REG_L	ra, 3*SZREG(sp)
-	REG_L	s0, 2*SZREG(sp)
-	REG_L	a0, 1*SZREG(sp)
-	REG_L	a1, 0*SZREG(sp)
-	addi	sp, sp, 4*SZREG
+	REG_L	ra, 1*SZREG(sp)
+	REG_L	s0, 8*SZREG(sp)
+	REG_L	a0, 10*SZREG(sp)
+	REG_L	a1, 11*SZREG(sp)
+	addi	sp, sp, ABI_SIZE_ON_STACK
 	.endm
 
 SYM_TYPED_FUNC_START(ftrace_stub)

arch/riscv/kernel/vector.c +8 -4

index a30fb2fb8a2b1..2afd5f926155b 100644
@@ -99,8 +99,8 @@ static bool insn_is_vector(u32 insn_buf)
 	return false;
 }
 
-static int riscv_v_thread_zalloc(struct kmem_cache *cache,
-				 struct __riscv_v_ext_state *ctx)
+static int riscv_v_thread_ctx_alloc(struct kmem_cache *cache,
+				    struct __riscv_v_ext_state *ctx)
 {
 	void *datap;

@@ -110,13 +110,15 @@ static int riscv_v_thread_zalloc(struct kmem_cache *cache,
 
 	ctx->datap = datap;
 	memset(ctx, 0, offsetof(struct __riscv_v_ext_state, datap));
+	ctx->vlenb = riscv_v_vsize / 32;
+
 	return 0;
 }
 
 void riscv_v_thread_alloc(struct task_struct *tsk)
 {
 #ifdef CONFIG_RISCV_ISA_V_PREEMPTIVE
-	riscv_v_thread_zalloc(riscv_v_kernel_cachep, &tsk->thread.kernel_vstate);
+	riscv_v_thread_ctx_alloc(riscv_v_kernel_cachep, &tsk->thread.kernel_vstate);
 #endif
 }

@@ -202,12 +204,14 @@ bool riscv_v_first_use_handler(struct pt_regs *regs)
 	 * context where VS has been off. So, try to allocate the user's V
 	 * context and resume execution.
 	 */
-	if (riscv_v_thread_zalloc(riscv_v_user_cachep, &current->thread.vstate)) {
+	if (riscv_v_thread_ctx_alloc(riscv_v_user_cachep, &current->thread.vstate)) {
 		force_sig(SIGBUS);
 		return true;
 	}
+
 	riscv_v_vstate_on(regs);
 	riscv_v_vstate_set_restore(current, regs);
+
 	return true;
 }

arch/s390/Kconfig +3 -2

index 5c9349df71ccf..5e6aebf1b739a 100644
@@ -184,7 +184,7 @@ config S390
 	select HAVE_FTRACE_MCOUNT_RECORD
 	select HAVE_FUNCTION_ARG_ACCESS_API
 	select HAVE_FUNCTION_ERROR_INJECTION
-	select HAVE_FUNCTION_GRAPH_RETVAL
+	select HAVE_FUNCTION_GRAPH_FREGS
 	select HAVE_FUNCTION_GRAPH_TRACER
 	select HAVE_FUNCTION_TRACER
 	select HAVE_GCC_PLUGINS

@@ -239,6 +239,7 @@ config S390
 	select SPARSE_IRQ
 	select SWIOTLB
 	select SYSCTL_EXCEPTION_TRACE
+	select SYSTEM_DATA_VERIFICATION if KEXEC_SIG
 	select THREAD_INFO_IN_TASK
 	select TRACE_IRQFLAGS_SUPPORT
 	select TTY

@@ -264,7 +265,7 @@ config ARCH_SUPPORTS_KEXEC_FILE
 	def_bool y
 
 config ARCH_SUPPORTS_KEXEC_SIG
-	def_bool MODULE_SIG_FORMAT
+	def_bool y
 
 config ARCH_SUPPORTS_KEXEC_PURGATORY
 	def_bool y

arch/s390/include/asm/ftrace.h +15 ~~-40~~

83 lines not on this page · raw message

arch/s390/kernel/asm-offsets.c +2 -8

index 3cfc4939033c9..8fd98a0f999f8 100644
@@ -179,14 +179,8 @@ int main(void)
 	DEFINE(OLDMEM_SIZE, PARMAREA + offsetof(struct parmarea, oldmem_size));
 	DEFINE(COMMAND_LINE, PARMAREA + offsetof(struct parmarea, command_line));
 	DEFINE(MAX_COMMAND_LINE_SIZE, PARMAREA + offsetof(struct parmarea, max_command_line_size));
-#ifdef CONFIG_FUNCTION_GRAPH_TRACER
-	/* function graph return value tracing */
-	OFFSET(__FGRAPH_RET_GPR2, fgraph_ret_regs, gpr2);
-	OFFSET(__FGRAPH_RET_FP, fgraph_ret_regs, fp);
-	DEFINE(__FGRAPH_RET_SIZE, sizeof(struct fgraph_ret_regs));
-#endif
-	OFFSET(__FTRACE_REGS_PT_REGS, ftrace_regs, regs);
-	DEFINE(__FTRACE_REGS_SIZE, sizeof(struct ftrace_regs));
+	OFFSET(__FTRACE_REGS_PT_REGS, __arch_ftrace_regs, regs);
+	DEFINE(__FTRACE_REGS_SIZE, sizeof(struct __arch_ftrace_regs));
 
 	OFFSET(__PCPU_FLAGS, pcpu, flags);
 	return 0;

arch/s390/kernel/ftrace.c +1 -1

index 0b6e62d1d8b87..51439a71e392c 100644
@@ -318,7 +318,7 @@ void kprobe_ftrace_handler(unsigned long ip, unsigned long parent_ip,
 	if (bit < 0)
 		return;
 
-	kmsan_unpoison_memory(fregs, sizeof(*fregs));
+	kmsan_unpoison_memory(fregs, ftrace_regs_size());
 	regs = ftrace_get_regs(fregs);
 	p = get_kprobe((kprobe_opcode_t *)ip);
 	if (!regs || unlikely(!p) || kprobe_disabled(p))

arch/s390/kernel/mcount.S +6 -6

index 7e267ef63a7fe..2b628aa3d8095 100644
@@ -134,14 +134,14 @@ SYM_CODE_END(ftrace_common)
 SYM_FUNC_START(return_to_handler)
 	stmg	%r2,%r5,32(%r15)
 	lgr	%r1,%r15
-	aghi	%r15,-(STACK_FRAME_OVERHEAD+__FGRAPH_RET_SIZE)
+	# allocate ftrace_regs and stack frame for ftrace_return_to_handler
+	aghi	%r15,-STACK_FRAME_SIZE_FREGS
 	stg	%r1,__SF_BACKCHAIN(%r15)
-	la	%r3,STACK_FRAME_OVERHEAD(%r15)
-	stg	%r1,__FGRAPH_RET_FP(%r3)
-	stg	%r2,__FGRAPH_RET_GPR2(%r3)
-	lgr	%r2,%r3
+	stg	%r2,(STACK_FREGS_PTREGS_GPRS+2*8)(%r15)
+	stg	%r1,(STACK_FREGS_PTREGS_GPRS+15*8)(%r15)
+	la	%r2,STACK_FRAME_OVERHEAD(%r15)
 	brasl	%r14,ftrace_return_to_handler
-	aghi	%r15,STACK_FRAME_OVERHEAD+__FGRAPH_RET_SIZE
+	aghi	%r15,STACK_FRAME_SIZE_FREGS
 	lgr	%r14,%r2
 	lmg	%r2,%r5,32(%r15)
 	BR_EX	%r14

arch/s390/kernel/perf_cpum_sf.c +1 -1

index efdd6ead7ba81..23a2a49547b7a 100644
@@ -856,7 +856,7 @@ static bool is_callchain_event(struct perf_event *event)
 	u64 sample_type = event->attr.sample_type;
 
 	return sample_type & (PERF_SAMPLE_CALLCHAIN | PERF_SAMPLE_REGS_USER |
-			      PERF_SAMPLE_STACK_USER);
+			      PERF_SAMPLE_REGS_INTR | PERF_SAMPLE_STACK_USER);
 }
 
 static int cpumsf_pmu_event_init(struct perf_event *event)

arch/s390/lib/test_unwind.c +2 -2

index 8b7f981e6f347..6e42100875e75 100644
@@ -270,9 +270,9 @@ static void notrace __used test_unwind_ftrace_handler(unsigned long ip,
 						      struct ftrace_ops *fops,
 						      struct ftrace_regs *fregs)
 {
-	struct unwindme *u = (struct unwindme *)fregs->regs.gprs[2];
+	struct unwindme *u = (struct unwindme *)arch_ftrace_regs(fregs)->regs.gprs[2];
 
-	u->ret = test_unwind(NULL, (u->flags & UWM_REGS) ? &fregs->regs : NULL,
+	u->ret = test_unwind(NULL, (u->flags & UWM_REGS) ? &arch_ftrace_regs(fregs)->regs : NULL,
 			     (u->flags & UWM_SP) ? u->sp : 0);
 }

arch/s390/pci/pci.c +17 -8

index 9e19d6076d3e8..2fe5b91c3d90f 100644
@@ -232,24 +232,33 @@ int zpci_fmb_disable_device(struct zpci_dev *zdev)
 static int zpci_cfg_load(struct zpci_dev *zdev, int offset, u32 *val, u8 len)
 {
 	u64 req = ZPCI_CREATE_REQ(zdev->fh, ZPCI_PCIAS_CFGSPC, len);
+	int rc = -ENODEV;
 	u64 data;
-	int rc;
+
+	if (!zdev_enabled(zdev))
+		goto out_err;
 
 	rc = __zpci_load(&data, req, offset);
-	if (!rc) {
-		data = le64_to_cpu((__force __le64) data);
-		data >>= (8 - len) * 8;
-		*val = (u32) data;
-	} else
-		*val = 0xffffffff;
+	if (rc)
+		goto out_err;
+	data = le64_to_cpu((__force __le64)data);
+	data >>= (8 - len) * 8;
+	*val = (u32)data;
+	return 0;
+
+out_err:
+	PCI_SET_ERROR_RESPONSE(val);
 	return rc;
 }
 
 static int zpci_cfg_store(struct zpci_dev *zdev, int offset, u32 val, u8 len)
 {
 	u64 req = ZPCI_CREATE_REQ(zdev->fh, ZPCI_PCIAS_CFGSPC, len);
+	int rc = -ENODEV;
 	u64 data = val;
-	int rc;
+
+	if (!zdev_enabled(zdev))
+		return rc;
 
 	data <<= (8 - len) * 8;
 	data = (__force u64) cpu_to_le64(data);

arch/s390/purgatory/Makefile +1 -0

index bdcf2a3b6c41b..df6636c8b492e 100644
@@ -21,6 +21,7 @@ KBUILD_CFLAGS += -fno-stack-protector
 KBUILD_CFLAGS += -DDISABLE_BRANCH_PROFILING
 KBUILD_CFLAGS += $(CLANG_FLAGS)
 KBUILD_CFLAGS += $(call cc-option,-fno-PIE)
+KBUILD_CFLAGS += $(call cc-option, -Wno-default-const-init-unsafe)
 KBUILD_AFLAGS := $(filter-out -DCC_USING_EXPOLINE,$(KBUILD_AFLAGS))
 
 # Since we link purgatory with -r unresolved symbols are not checked, so we

arch/sparc/include/uapi/asm/ioctls.h +4 -4

index 7fd2f5873c9e7..a8bbdf9877a41 100644
@@ -5,10 +5,10 @@
 #include <asm/ioctl.h>
 
 /* Big T */
-#define TCGETA		_IOR('T', 1, struct termio)
-#define TCSETA		_IOW('T', 2, struct termio)
-#define TCSETAW		_IOW('T', 3, struct termio)
-#define TCSETAF		_IOW('T', 4, struct termio)
+#define TCGETA          0x40125401 /* _IOR('T', 1, struct termio) */
+#define TCSETA          0x80125402 /* _IOW('T', 2, struct termio) */
+#define TCSETAW         0x80125403 /* _IOW('T', 3, struct termio) */
+#define TCSETAF         0x80125404 /* _IOW('T', 4, struct termio) */
 #define TCSBRK		_IO('T', 5)
 #define TCXONC		_IO('T', 6)
 #define TCFLSH		_IO('T', 7)

arch/sparc/kernel/process.c +24 ~~-14~~

index 0442ab00518d3..7d69877511fac 100644
@@ -17,14 +17,18 @@
 
 asmlinkage long sparc_fork(struct pt_regs *regs)
 {
-	unsigned long orig_i1 = regs->u_regs[UREG_I1];
+	unsigned long orig_i1;
 	long ret;
 	struct kernel_clone_args args = {
 		.exit_signal	= SIGCHLD,
-		/* Reuse the parent's stack for the child. */
-		.stack		= regs->u_regs[UREG_FP],
 	};
 
+	synchronize_user_stack();
+
+	orig_i1 = regs->u_regs[UREG_I1];
+	/* Reuse the parent's stack for the child. */
+	args.stack = regs->u_regs[UREG_FP];
+
 	ret = kernel_clone(&args);
 
 	/* If we get an error and potentially restart the system

@@ -40,16 +44,19 @@ asmlinkage long sparc_fork(struct pt_regs *regs)
 
 asmlinkage long sparc_vfork(struct pt_regs *regs)
 {
-	unsigned long orig_i1 = regs->u_regs[UREG_I1];
+	unsigned long orig_i1;
 	long ret;
-
 	struct kernel_clone_args args = {
 		.flags		= CLONE_VFORK | CLONE_VM,
 		.exit_signal	= SIGCHLD,
-		/* Reuse the parent's stack for the child. */
-		.stack		= regs->u_regs[UREG_FP],
 	};
 
+	synchronize_user_stack();
+
+	orig_i1 = regs->u_regs[UREG_I1];
+	/* Reuse the parent's stack for the child. */
+	args.stack = regs->u_regs[UREG_FP];
+
 	ret = kernel_clone(&args);
 
 	/* If we get an error and potentially restart the system

@@ -65,15 +72,18 @@ asmlinkage long sparc_vfork(struct pt_regs *regs)
 
 asmlinkage long sparc_clone(struct pt_regs *regs)
 {
-	unsigned long orig_i1 = regs->u_regs[UREG_I1];
-	unsigned int flags = lower_32_bits(regs->u_regs[UREG_I0]);
+	unsigned long orig_i1;
+	unsigned int flags;
 	long ret;
+	struct kernel_clone_args args = {0};
 
-	struct kernel_clone_args args = {
-		.flags		= (flags & ~CSIGNAL),
-		.exit_signal	= (flags & CSIGNAL),
-		.tls		= regs->u_regs[UREG_I3],
-	};
+	synchronize_user_stack();
+
+	orig_i1 = regs->u_regs[UREG_I1];
+	flags = lower_32_bits(regs->u_regs[UREG_I0]);
+	args.flags		= (flags & ~CSIGNAL);
+	args.exit_signal	= (flags & CSIGNAL);
+	args.tls		= regs->u_regs[UREG_I3];
 
 #ifdef CONFIG_COMPAT
 	if (test_thread_flag(TIF_32BIT)) {

arch/x86/Kconfig +1 -1

index df14d0e67ea0c..d1c73d5ed32f7 100644
@@ -231,7 +231,7 @@ config X86
 	select HAVE_GUP_FAST
 	select HAVE_FENTRY			if X86_64 || DYNAMIC_FTRACE
 	select HAVE_FTRACE_MCOUNT_RECORD
-	select HAVE_FUNCTION_GRAPH_RETVAL	if HAVE_FUNCTION_GRAPH_TRACER
+	select HAVE_FUNCTION_GRAPH_FREGS	if HAVE_FUNCTION_GRAPH_TRACER
 	select HAVE_FUNCTION_GRAPH_TRACER	if X86_32 || (X86_64 && DYNAMIC_FTRACE)
 	select HAVE_FUNCTION_TRACER
 	select HAVE_GCC_PLUGINS

arch/x86/events/core.c +2 -2

index 86ba035f17a35..0f935cced0b7d 100644
@@ -3051,8 +3051,8 @@ void perf_get_x86_pmu_capability(struct x86_pmu_capability *cap)
 	cap->version		= x86_pmu.version;
 	cap->num_counters_gp	= x86_pmu_num_counters(NULL);
 	cap->num_counters_fixed	= x86_pmu_num_counters_fixed(NULL);
-	cap->bit_width_gp	= x86_pmu.cntval_bits;
-	cap->bit_width_fixed	= x86_pmu.cntval_bits;
+	cap->bit_width_gp	= cap->num_counters_gp ? x86_pmu.cntval_bits : 0;
+	cap->bit_width_fixed	= cap->num_counters_fixed ? x86_pmu.cntval_bits : 0;
 	cap->events_mask	= (unsigned int)x86_pmu.events_maskl;
 	cap->events_mask_len	= x86_pmu.events_mask_len;
 	cap->pebs_ept		= x86_pmu.pebs_ept;

arch/x86/events/intel/cstate.c +1 -0

index aee2dfc108408..05bc2b799dd29 100644
@@ -597,6 +597,7 @@ static const struct x86_cpu_id intel_cstates_match[] __initconst = {
 	X86_MATCH_VFM(INTEL_ATOM_SILVERMONT,	&slm_cstates),
 	X86_MATCH_VFM(INTEL_ATOM_SILVERMONT_D,	&slm_cstates),
 	X86_MATCH_VFM(INTEL_ATOM_AIRMONT,	&slm_cstates),
+	X86_MATCH_VFM(INTEL_ATOM_AIRMONT_NP,	&slm_cstates),
 
 	X86_MATCH_VFM(INTEL_BROADWELL,		&snb_cstates),
 	X86_MATCH_VFM(INTEL_BROADWELL_D,	&snb_cstates),

arch/x86/events/msr.c +1 -0

index 45b1866ff0513..3a05ea2871dc5 100644
@@ -76,6 +76,7 @@ static bool test_intel(int idx, void *data)
 	case INTEL_ATOM_SILVERMONT:
 	case INTEL_ATOM_SILVERMONT_D:
 	case INTEL_ATOM_AIRMONT:
+	case INTEL_ATOM_AIRMONT_NP:
 
 	case INTEL_ATOM_GOLDMONT:
 	case INTEL_ATOM_GOLDMONT_D:

arch/x86/hyperv/hv_vtl.c +5 -3

index 2510e91b29b08..b135ba5c18710 100644
@@ -68,7 +68,7 @@ static void hv_vtl_ap_entry(void)
 
 static int hv_vtl_bringup_vcpu(u32 target_vp_index, int cpu, u64 eip_ignored)
 {
-	u64 status;
+	u64 status, rsp, rip;
 	int ret = 0;
 	struct hv_enable_vp_vtl *input;
 	unsigned long irq_flags;

@@ -81,9 +81,11 @@ static int hv_vtl_bringup_vcpu(u32 target_vp_index, int cpu, u64 eip_ignored)
 	struct desc_struct *gdt;
 
 	struct task_struct *idle = idle_thread_get(cpu);
-	u64 rsp = (unsigned long)idle->thread.sp;
+	if (IS_ERR(idle))
+		return PTR_ERR(idle);
 
-	u64 rip = (u64)&hv_vtl_ap_entry;
+	rsp = (unsigned long)idle->thread.sp;
+	rip = (u64)&hv_vtl_ap_entry;
 
 	native_store_gdt(&gdt_ptr);
 	store_idt(&idt_ptr);

arch/x86/include/asm/ftrace.h +19 ~~-43~~

87 lines not on this page · raw message

arch/x86/kernel/ftrace.c +1 -1

index bfab966ea56e8..d3b14a9ad2edb 100644
@@ -647,7 +647,7 @@ void prepare_ftrace_return(unsigned long ip, unsigned long *parent,
 void ftrace_graph_func(unsigned long ip, unsigned long parent_ip,
 		       struct ftrace_ops *op, struct ftrace_regs *fregs)
 {
-	struct pt_regs *regs = &fregs->regs;
+	struct pt_regs *regs = &arch_ftrace_regs(fregs)->regs;
 	unsigned long *stack = (unsigned long *)kernel_stack_pointer(regs);
 
 	prepare_ftrace_return(ip, (unsigned long *)stack, 0);

arch/x86/kernel/ftrace_32.S +7 -6

index 58d9ed50fe617..f4e0c33612342 100644
@@ -187,14 +187,15 @@ SYM_CODE_END(ftrace_graph_caller)
 
 .globl return_to_handler
 return_to_handler:
-	pushl	$0
-	pushl	%edx
-	pushl	%eax
+	subl	$(PTREGS_SIZE), %esp
+	movl	$0, PT_EBP(%esp)
+	movl	%edx, PT_EDX(%esp)
+	movl	%eax, PT_EAX(%esp)
 	movl	%esp, %eax
 	call	ftrace_return_to_handler
 	movl	%eax, %ecx
-	popl	%eax
-	popl	%edx
-	addl	$4, %esp		# skip ebp
+	movl	PT_EAX(%esp), %eax
+	movl	PT_EDX(%esp), %edx
+	addl	$(PTREGS_SIZE), %esp
 	JMP_NOSPEC ecx
 #endif

arch/x86/kernel/ftrace_64.S +15 -8

index 214f30e9f0c01..8a3cff618692c 100644
@@ -348,21 +348,28 @@ STACK_FRAME_NON_STANDARD_FP(__fentry__)
 SYM_CODE_START(return_to_handler)
 	UNWIND_HINT_UNDEFINED
 	ANNOTATE_NOENDBR
-	subq  $24, %rsp
 
-	/* Save the return values */
-	movq %rax, (%rsp)
-	movq %rdx, 8(%rsp)
-	movq %rbp, 16(%rsp)
+	/* Restore return_to_handler value that got eaten by previous ret instruction. */
+	subq $8, %rsp
+	UNWIND_HINT_FUNC
+
+	/* Save ftrace_regs for function exit context  */
+	subq $(FRAME_SIZE), %rsp
+
+	movq %rax, RAX(%rsp)
+	movq %rdx, RDX(%rsp)
+	movq %rbp, RBP(%rsp)
+	movq %rsp, RSP(%rsp)
 	movq %rsp, %rdi
 
 	call ftrace_return_to_handler
 
 	movq %rax, %rdi
-	movq 8(%rsp), %rdx
-	movq (%rsp), %rax
+	movq RDX(%rsp), %rdx
+	movq RAX(%rsp), %rax
+
+	addq $(FRAME_SIZE) + 8, %rsp
 
-	addq $24, %rsp
 	/*
 	 * Jump back to the old return address. This cannot be JMP_NOSPEC rdi
 	 * since IBT would demand that contain ENDBR, which simply isn't so for

arch/x86/kernel/kexec-bzimage64.c +7 -0

index 68530fad05f74..c776b01e87898 100644
@@ -184,6 +184,13 @@ setup_efi_state(struct boot_params *params, unsigned long params_load_addr,
 	struct efi_info *current_ei = &boot_params.efi_info;
 	struct efi_info *ei = &params->efi_info;
 
+	if (!params->acpi_rsdp_addr) {
+		if (efi.acpi20 != EFI_INVALID_TABLE_ADDR)
+			params->acpi_rsdp_addr = efi.acpi20;
+		else if (efi.acpi != EFI_INVALID_TABLE_ADDR)
+			params->acpi_rsdp_addr = efi.acpi;
+	}
+
 	if (!efi_enabled(EFI_RUNTIME_SERVICES))
 		return 0;

arch/x86/kernel/setup.c +6 -0

index f1fea506e20f4..234c4d9e50b8f 100644
@@ -372,9 +372,15 @@ int __init ima_free_kexec_buffer(void)
 
 int __init ima_get_kexec_buffer(void **addr, size_t *size)
 {
+	int ret;
+
 	if (!ima_kexec_buffer_size)
 		return -ENOENT;
 
+	ret = ima_validate_range(ima_kexec_buffer_phys, ima_kexec_buffer_size);
+	if (ret)
+		return ret;
+
 	*addr = __va(ima_kexec_buffer_phys);
 	*size = ima_kexec_buffer_size;

arch/x86/kvm/svm/nested.c +1 -2

index c6556599376e2..862758eeac846 100644
@@ -1760,10 +1760,9 @@ static int svm_set_nested_state(struct kvm_vcpu *vcpu,
 	 * thus MMU might not be initialized correctly.
 	 * Set it again to fix this.
 	 */
-
 	ret = nested_svm_load_cr3(&svm->vcpu, vcpu->arch.cr3,
 				  nested_npt_enabled(svm), false);
-	if (WARN_ON_ONCE(ret))
+	if (ret)
 		goto out_free;
 
 	svm->nested.force_msr_bitmap_recalc = true;

arch/x86/kvm/svm/svm.c +3 -2

index 85816c4186b96..853a86dfc8f1b 100644
@@ -2358,12 +2358,13 @@ static int vmload_vmsave_interception(struct kvm_vcpu *vcpu, bool vmload)
 
 	ret = kvm_skip_emulated_instruction(vcpu);
 
+	/* KVM always performs VMLOAD/VMSAVE on VMCB01 (see __svm_vcpu_run()) */
 	if (vmload) {
-		svm_copy_vmloadsave_state(svm->vmcb, vmcb12);
+		svm_copy_vmloadsave_state(svm->vmcb01.ptr, vmcb12);
 		svm->sysenter_eip_hi = 0;
 		svm->sysenter_esp_hi = 0;
 	} else {
-		svm_copy_vmloadsave_state(vmcb12, svm->vmcb);
+		svm_copy_vmloadsave_state(vmcb12, svm->vmcb01.ptr);
 	}
 
 	kvm_vcpu_unmap(vcpu, &map, true);

arch/x86/kvm/x86.c +22 ~~-20~~

120 lines not on this page · raw message

arch/x86/platform/pvh/head.S +2 -0

index ce4fd8d33da46..2774cf74fa940 100644

Lines of this file are not shown. View the raw message.

arch/x86/xen/enlighten.c +1 -1

index 0c950bbca309f..86dd33f1aeaab 100644

Lines of this file are not shown. View the raw message.

block/bio.c +16 -0

index 094a5adf79d23..b919f3fa2f2d4 100644

Lines of this file are not shown. View the raw message.

block/blk-merge.c +17 -4

index 7ddd7dd23dda8..68dc8076d8cbc 100644

Lines of this file are not shown. View the raw message.

block/blk-mq-debugfs.c +2 -0

index 5463697a84428..cbc8bbde3a2bb 100644

Lines of this file are not shown. View the raw message.

block/blk.h +5 -1

index 63c92db0a5079..e7d7c5c636524 100644

Lines of this file are not shown. View the raw message.

drivers/acpi/acpi_processor.c +15 ~~-13~~

index 2a99f5eb69629..d8674aee28c2e 100644

Lines of this file are not shown. View the raw message.

drivers/acpi/acpica/evregion.c +3 -1

index cf53b9535f18e..7788c27ccf461 100644

Lines of this file are not shown. View the raw message.

drivers/acpi/acpica/exoparg3.c +18 ~~-28~~

46 lines not on this page · raw message

drivers/acpi/apei/ghes.c +33 -5

index 45fa2510e4cf5..98901fbe2f7b7 100644

Lines of this file are not shown. View the raw message.

drivers/acpi/battery.c +8 -1

index 11c7e35fafa25..a33d60e625f81 100644

Lines of this file are not shown. View the raw message.

drivers/acpi/cppc_acpi.c +2 -2

index 1e8e2002f81af..c90121cae628a 100644

Lines of this file are not shown. View the raw message.

drivers/acpi/power.c +13 -0

index c2c70139c4f1d..ff5fcd541e50f 100644

Lines of this file are not shown. View the raw message.

drivers/acpi/resource.c +8 -0

index 4937032490689..8a01a3718aa94 100644

Lines of this file are not shown. View the raw message.

drivers/acpi/x86/s2idle.c +6 -0

index dd0b40b9bbe8b..377a268867c21 100644

Lines of this file are not shown. View the raw message.

drivers/acpi/x86/utils.c +12 -0

index 4ee30c2897a2b..418951639f511 100644

Lines of this file are not shown. View the raw message.

drivers/android/binder.c +1 -1

index 9a6d1822dc3be..c470f5cce9911 100644

Lines of this file are not shown. View the raw message.

drivers/android/binder_alloc.c +3 -3

index b3acbc4174fb1..7556f470f921b 100644

Lines of this file are not shown. View the raw message.

drivers/ata/libata-core.c +24 -0

index 33454d01c2044..39dcefb1fdd54 100644

Lines of this file are not shown. View the raw message.

drivers/ata/libata-eh.c +2 -1

index 16cd676eae1f9..205c62cf9e32d 100644

Lines of this file are not shown. View the raw message.

drivers/ata/libata-scsi.c +53 ~~-31~~

84 lines not on this page · raw message

drivers/ata/libata.h +1 -0

index 0337be4faec7c..d07693bd054eb 100644

Lines of this file are not shown. View the raw message.

drivers/ata/pata_ftide010.c +3 -3

index 73a9a5109238b..01f03031315aa 100644

Lines of this file are not shown. View the raw message.

drivers/atm/fore200e.c +4 -0

index e815d58f7c955..c18a88ccd8cc3 100644

Lines of this file are not shown. View the raw message.

drivers/auxdisplay/arm-charlcd.c +1 -1

index a7eae99a48f77..4e22882f57c9c 100644

Lines of this file are not shown. View the raw message.

drivers/base/power/wakeirq.c +6 -3

index 5a5a9e978e85f..ddbe9cc91d23d 100644

Lines of this file are not shown. View the raw message.

drivers/base/power/wakeup.c +1 -3

index 752b417e81290..706cd556a0d69 100644

Lines of this file are not shown. View the raw message.

drivers/block/drbd/drbd_main.c +0 -3

index 5bbd312c3e14d..8c5a7bcfa82b2 100644

Lines of this file are not shown. View the raw message.

drivers/block/drbd/drbd_nl.c +19 -1

index 720fc30e2ecc9..8c12bf1b2a0d2 100644

Lines of this file are not shown. View the raw message.

drivers/block/rnbd/rnbd-srv.c +24 ~~-13~~

index 08ce6d96d04cf..0c7d40ed8d199 100644

Lines of this file are not shown. View the raw message.

drivers/block/ublk_drv.c +3 -3

index 2d46383e8d26b..c6a59f02944fc 100644

Lines of this file are not shown. View the raw message.

drivers/bluetooth/btintel_pcie.c +2 -7

index 34812bf7587d6..d430645657e3d 100644

Lines of this file are not shown. View the raw message.

drivers/bluetooth/btusb.c +5 -0

index 490efe4d67a97..9d3236321056b 100644

Lines of this file are not shown. View the raw message.

drivers/bluetooth/hci_qca.c +14 ~~-10~~

index e6ad01d5e1d5d..586a2ff72a2ae 100644

Lines of this file are not shown. View the raw message.

drivers/bus/fsl-mc/fsl-mc-bus.c +1 -5

index bdf78260929d9..5543ba93e5017 100644

Lines of this file are not shown. View the raw message.

drivers/bus/omap-ocp2scp.c +2 ~~-11~~

index 7d7479ba0a759..87e290a3dc817 100644

Lines of this file are not shown. View the raw message.

drivers/char/hw_random/core.c +109 ~~-64~~

173 lines not on this page · raw message

drivers/char/ipmi/ipmi_ipmb.c +5 -0

index 6a4f279c7c1f5..163ec867d68af 100644

Lines of this file are not shown. View the raw message.

drivers/char/random.c +1 ~~-11~~

index 23ee76bbb4aa7..a23c8b2feab6c 100644

Lines of this file are not shown. View the raw message.

drivers/char/tpm/st33zp24/st33zp24.c +4 -2

index c0771980bc2ff..06caf53a42ee5 100644

Lines of this file are not shown. View the raw message.

drivers/char/tpm/tpm_i2c_infineon.c +4 -2

index 81d8a78dc6552..3675faa4a00c7 100644

Lines of this file are not shown. View the raw message.

drivers/char/tpm/tpm_tis_i2c_cr50.c +1 -2

index adf22992138e5..d51ef9c880832 100644

Lines of this file are not shown. View the raw message.

drivers/char/tpm/tpm_tis_spi_cr50.c +1 -1

index f4937280e9406..32920b4cecfb4 100644

Lines of this file are not shown. View the raw message.

drivers/clk/clk-apple-nco.c +1 -0

index 457a48d489412..c205b7f1dadeb 100644

Lines of this file are not shown. View the raw message.

drivers/clk/clk-renesas-pcie.c +1 -1

index 4c3a5e4eb77ac..f94a9c4d0b670 100644

Lines of this file are not shown. View the raw message.

drivers/clk/mediatek/clk-mtk.c +7 -5

index ba1d1c495bc2b..644e5a854f2b6 100644

Lines of this file are not shown. View the raw message.

drivers/clk/meson/gxbb.c +14 -3

index d9529de200ae4..2bfb0ab9c93cc 100644

Lines of this file are not shown. View the raw message.

drivers/clk/microchip/clk-core.c +12 ~~-13~~

index 1b4f023cdc8be..71fbaf8318f22 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/clk-rcg2.c +3 -4

index bf6406f5279a4..6aa9dcdabffde 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/common.c +1 -1

index cab2dbb7a8d49..e1a83ec481509 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/dispcc-sdm845.c +2 -2

index e6139e8f74dc0..1859c093a241b 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/dispcc-sm7150.c +1 -1

index 1e2a98a63511d..3cd2af842143c 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/gcc-ipq5018.c +1 -0

index 24eb4c40da634..ee45ba9f13e06 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/gcc-msm8917.c +0 -1

index 3e2a2ae2ee6e9..cb5e18b084296 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/gcc-msm8953.c +0 -1

index 8f29ecc74c50b..8fe1d3e421440 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/gcc-qdu1000.c +2 -2

index dbe9e9437939a..915bb9b4ff813 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/gcc-sdx75.c +2 -2

index 453a6bf8e8786..1f3cd58483a2d 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/gcc-sm4450.c +3 -3

index e2d9e4691c5b7..023d840e9f4ef 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/gcc-sm8450.c +2 -2

index c445c271678a5..ff62381ecdd97 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/gcc-sm8550.c +2 -2

index 862a9bf73bcb5..36a5b7de5b55d 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/gcc-sm8650.c +2 -2

index fa1672c4e7d81..8c4b86494183c 100644

Lines of this file are not shown. View the raw message.

drivers/clk/qcom/gcc-x1e80100.c +2 -2

index 86cc8ecf16a48..0c49f0461ae32 100644

Lines of this file are not shown. View the raw message.

drivers/clk/renesas/rzg2l-cpg.c +3 -3

index e4f2d974f38a1..214a9e89379ae 100644

Lines of this file are not shown. View the raw message.

drivers/clk/tegra/clk-tegra124-emc.c +3 -1

index 2a6db04342815..0f6fb776b2298 100644

Lines of this file are not shown. View the raw message.

drivers/clocksource/Kconfig +1 -0

index d546903dba4f3..abfc2aa857678 100644

Lines of this file are not shown. View the raw message.

drivers/clocksource/sh_tmu.c +0 ~~-18~~

index beffff81c00f3..3fc6ed9b56300 100644

Lines of this file are not shown. View the raw message.

drivers/cpufreq/cpufreq-dt-platdev.c +3 -0

index dbd73cd0cf535..9e86a0e8b9e86 100644

Lines of this file are not shown. View the raw message.

drivers/cpufreq/intel_pstate.c +1 -1

index 9d8cb44c26c70..f8f9ff2b73ea0 100644

Lines of this file are not shown. View the raw message.

drivers/cpufreq/scmi-cpufreq.c +1 -0

index bb265541671a5..f6aee1f28ab88 100644

Lines of this file are not shown. View the raw message.

drivers/cpuidle/cpuidle.c +10 -0

index 0e1bbc966135d..2cb11e5a11251 100644

Lines of this file are not shown. View the raw message.

drivers/cpuidle/governors/menu.c +11 ~~-11~~

index 3be761961f1be..0ce7323450011 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/caam/caamalg_qi2.c +15 ~~-12~~

index e809d030ab113..ece9f1e5a689f 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/caam/caamalg_qi2.h +2 -0

index 61d1219a202fc..8e65b4b28c7ba 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/cavium/cpt/cptvf_main.c +2 -1

index c246920e6f540..bccd680c7f7ee 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/ccp/psp-dev.c +11 -0

index 1c5a7189631ec..fa43da7824207 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/ccp/sev-dev.c +119 ~~-34~~

153 lines not on this page · raw message

drivers/crypto/ccp/sp-dev.c +12 -0

index 7eb3e46682860..ccbe009ad6e58 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/ccp/sp-dev.h +3 -0

index 6f9d7063257d7..c8a611ef275b5 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/ccp/sp-pci.c +15 -1

index 224edaaa737b6..e8f7fcf66cc72 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/ccp/tee-dev.c +44 ~~-12~~

56 lines not on this page · raw message

drivers/crypto/ccp/tee-dev.h +1 -0

index ea9a2b7c05f57..c23416cb7bb37 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/hisilicon/qm.c +5 -1

index d0b154d13f445..2c64bf4cdf0dc 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/hisilicon/sec2/sec_crypto.c +47 ~~-15~~

62 lines not on this page · raw message

drivers/crypto/hisilicon/trng/trng.c +86 ~~-35~~

121 lines not on this page · raw message

drivers/crypto/hisilicon/zip/zip_crypto.c +9 ~~-15~~

index 7327f8f29b013..42ac275be36fc 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/intel/qat/qat_common/adf_pfvf_pf_proto.c +10 -0

index b9b5e744a3f16..af8dbc7517cf8 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/marvell/octeontx/otx_cptvf_main.c +2 -1

index 88a41d1ca5f64..6c0bfb3ea1c9f 100644

Lines of this file are not shown. View the raw message.

drivers/crypto/starfive/jh7110-aes.c +7 -2

index 86a1a1fa9f8f9..04f2f97ce238a 100644

Lines of this file are not shown. View the raw message.

drivers/cxl/core/hdm.c +1 -2

index 223c273c0cd17..fde609f37e562 100644

Lines of this file are not shown. View the raw message.

drivers/dma/dma-axi-dmac.c +4 -7

index 36943b0c6d603..47d95d2d743b1 100644

Lines of this file are not shown. View the raw message.

drivers/dma/fsl-edma-main.c +0 -1

index 4794d58dab556..540b47c520dce 100644

Lines of this file are not shown. View the raw message.

drivers/dma/mediatek/mtk-uart-apdma.c +5 -5

index 1bdc1500be40f..3e7f8acf41dd0 100644

Lines of this file are not shown. View the raw message.

drivers/dma/stm32/stm32-dma3.c +1 -6

index 0be6e944df6fd..fde1b10d3532c 100644

Lines of this file are not shown. View the raw message.

drivers/dma/stm32/stm32-mdma.c +1 -1

index e6d525901de7e..3560a6945fbfc 100644

Lines of this file are not shown. View the raw message.

drivers/dma/sun6i-dma.c +20 -6

index 583bf49031cf2..c97027379263d 100644

Lines of this file are not shown. View the raw message.

drivers/edac/altera_edac.c +4 -7

index 3bb851e1e608a..6c5fb06976415 100644

Lines of this file are not shown. View the raw message.

drivers/edac/i5000_edac.c +1 -0

index 4b5a71f8739d9..8c6a291e01f6a 100644

Lines of this file are not shown. View the raw message.

drivers/edac/i5400_edac.c +1 -1

index 49b4499269fb7..68afb3bb8e290 100644

Lines of this file are not shown. View the raw message.

drivers/firmware/arm_ffa/driver.c +30 -4

index 9fdfccbc6479a..9516ee870cd25 100644

Lines of this file are not shown. View the raw message.

drivers/firmware/efi/cper-arm.c +8 -4

index 52d18490b59e3..70e1735dfcdd4 100644

Lines of this file are not shown. View the raw message.

drivers/firmware/efi/cper.c +7 -1

index 16b27fe9608fd..3587295cd0206 100644

Lines of this file are not shown. View the raw message.

drivers/firmware/efi/efi.c +4 -4

index acabc856fe8a5..0d1a65879a358 100644

Lines of this file are not shown. View the raw message.

drivers/fpga/dfl.c +1 -1

index c406b949026fa..c6bad1d2d2ae4 100644

Lines of this file are not shown. View the raw message.

drivers/fpga/of-fpga-region.c +4 -4

index 8526a5a86f0cb..efc35dad6aaa3 100644

Lines of this file are not shown. View the raw message.

drivers/gpio/gpio-aspeed-sgpio.c +3 -2

index 72755fee64784..e69a6ce7be3fb 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/amdgpu_acpi.c +3 -1

index bebfbc1497d8e..d484804181756 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/amdgpu_device.c +2 -1

index 1cf90557b310b..cab75f5c9f2fd 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/amdgpu_discovery.c +1 -0

index e09db65880e1a..f62ac736ed76c 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/amdgpu_dma_buf.c +8 -1

index 9d79f1cc6a19b..951ab989d668b 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/amdgpu_drv.c +0 -1

index 48de2f088a3b9..bf706ee2e0ed3 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/amdgpu_gmc.c +11 -1

index f159641271672..564c68c9277b3 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/amdgpu_job.c +2 -1

index 7e6057a6e7f17..ba9a9adca0bff 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/amdgpu_psp.c +1 -1

index fa84208eed18e..26260873f6a15 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/amdgpu_ras.c +1 -1

index d9cdc89d4cde1..bf563904b3fa9 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/amdgpu_virt.c +1 -0

index 9247cd7b1868c..78af6e9282256 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdgpu/vcn_v2_0.c +23 ~~-22~~

45 lines not on this page · raw message

drivers/gpu/drm/amd/amdkfd/kfd_debug.c +12 -8

index a8abc30918013..3a8df47aa5821 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdkfd/kfd_events.c +6 -0

index 6798510c4a707..4e5ae56562838 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdkfd/kfd_migrate.c +1 -1

index f31e9fbf634a0..52246f16cc242 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdkfd/kfd_process.c +1 -1

index 45923da7709fd..64f3a0687f8a2 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdkfd/kfd_queue.c +3 -3

index 0c6ef2919d870..1f1169a4d1540 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/amdkfd/kfd_svm.c +6 -1

index d65b0b23ec7b8..7f2dbb6c2cbf8 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/amdgpu_dm/amdgpu_dm.c +35 -9

44 lines not on this page · raw message

drivers/gpu/drm/amd/display/amdgpu_dm/amdgpu_dm_plane.c +7 -2

index 62e30942f735d..1e993f5d734a6 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/clk_mgr/dcn35/dcn35_clk_mgr.c +8 -8

index 6e9d6090b10ff..33ee7e81b1b93 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/dio/dcn32/dcn32_dio_link_encoder.c +12 -3

index 06907e8a4eda1..ddc736af776c9 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/dml/dcn35/dcn35_fpu.c +2 -2

index c90dee4e9116a..c15bd05def93f 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/dpp/dcn30/dcn30_dpp.c +18 -3

index 6c3cae593ad54..ba12c294f971a 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/dpp/dcn30/dcn30_dpp.h +4 -0

index b110f35ef66bd..d183875b13302 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/dpp/dcn401/dcn401_dpp.c +3 -3

index 97bf26fa35738..3e24ac07eebd9 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/hwss/dce110/dce110_hwseq.c +24 ~~-12~~

index 31c7dfff27cbb..df69e0cebf785 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/hwss/dcn20/dcn20_hwseq.c +10 -2

index b94fe14f4b935..a113085385d15 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/hwss/dcn401/dcn401_hwseq.c +5 -3

index f805803be55e4..e62d415b16004 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/mpc/dcn32/dcn32_mpc.c +1 -2

index a0e9e9f0441a4..acf726137488d 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/resource/dcn315/dcn315_resource.c +4 -4

index 9cb72805b8d1a..ad3f229f39cba 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/resource/dcn316/dcn316_resource.c +4 -4

index af82e13029c9e..b2d8383411b21 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/resource/dcn32/dcn32_resource.c +4 -4

index 6b889c8be0ca3..62dbb0f3073c0 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/resource/dcn321/dcn321_resource.c +4 -4

index 74113c578bac4..84aaa7a5ae30f 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/resource/dcn35/dcn35_resource.c +4 -4

index 92d5e3252d2d4..90d63e3174344 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/display/dc/resource/dcn351/dcn351_resource.c +4 -4

index 6e27226cec289..9c72e87b606a2 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/amd/pm/legacy-dpm/si_dpm.c +5 -0

index 29cecfab07042..37a91a76208e5 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/atmel-hlcdc/atmel_hlcdc_plane.c +6 ~~-19~~

index 3787db014501e..ae8d7b017968d 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/bridge/analogix/anx7625.c +1 -1

index 7244c3abb7f99..3273c368b8357 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/display/drm_dp_mst_topology.c +2 -1

index 3e5f721d75400..997f2489f00f3 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/drm_buddy.c +10 -0

index 7debf079c943f..adfcdd5645d9a 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/drm_property.c +1 -1

index 596272149a359..3c88b5fbdf28c 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/i915/display/intel_acpi.c +1 -0

index c3b29a331d725..859fedb9d93ea 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/i915/intel_wakeref.c +1 -1

index dea2f63184f89..40fbf2ccaee21 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/i915/intel_wakeref.h +5 -9

index 68aa3be482515..ca4c4a91a49fd 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/msm/adreno/a2xx_gpu.c +4 -1

index 2e25af3462ab6..a0ca41f4818a3 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/msm/disp/dpu1/catalog/dpu_7_2_sc7280.h +12 -2

index 2f153e0b5c6a9..d53ab3d886262 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/msm/disp/dpu1/dpu_encoder.c +9 -9

index 47b514c89ce66..170d60bb7602d 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/msm/disp/dpu1/dpu_encoder_phys_cmd.c +4 -3

index 6fc31d47cd1dc..65dad86edb46e 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/msm/disp/dpu1/dpu_hw_intf.c +46 -3

49 lines not on this page · raw message

drivers/gpu/drm/msm/disp/dpu1/dpu_hw_intf.h +2 -1

index fc23650dfbf05..4039f11068764 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/msm/disp/dpu1/dpu_hw_top.c +0 -7

index 2040bee8d512f..2c312439cf184 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/msm/disp/dpu1/dpu_hw_util.h +7 -0

index 67b08e99335dc..6fe65bc3bff4e 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/msm/disp/mdp_format.c +4 -4

index 426782d50cb49..eebedb1a2636e 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/panel/panel-edp.c +1 -0

index 663af985d1b38..d6806956f63e9 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/panel/panel-jdi-lpm102a188a.c +3 -1

index 5b5082efb282b..eba560e422e8b 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/panel/panel-lg-sw43408.c +0 -4

index f3dcc39670eae..8109ded2fe563 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/panthor/panthor_gpu.c +12 -7

index 1ca2924e6d552..15e4371d98945 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/panthor/panthor_mmu.c +4 -0

index ed769749ec354..e221708cf1aa3 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/panthor/panthor_sched.c +107 ~~-60~~

167 lines not on this page · raw message

drivers/gpu/drm/panthor/panthor_sched.h +1 -0

index 3a30d2328b308..666d1655ee18e 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/radeon/si_dpm.c +5 -0

index 9deb91970d4df..f12227145ef08 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/tests/drm_gem_shmem_test.c +3 -3

index 925fbc2cda700..0c8c46ca158c0 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/v3d/v3d_drv.c +2 -0

index 7c17108da7d2d..f45fdd7d542f6 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_assert.h +1 -1

index e22bbf57fca75..04d6b95c6d878 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_device.c +1 -0

index 161c73e676640..3ce5bf902f700 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_device.h +2 -1

index 34620ef855c0c..5dad24fc487ca 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_device_types.h +41 ~~-15~~

56 lines not on this page · raw message

drivers/gpu/drm/xe/xe_gt_freq.c +1 -1

index a05fde2c7b122..62a8aa2fdbb0d 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_gt_printk.h +1 -1

index d6228baaff1ef..5dc71394372d6 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_gt_types.h +12 ~~-10~~

index 3d1c51de02687..a287b98ee70b4 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_guc_submit.c +2 -1

index f316be1e96452..d0ef3a6a68d2c 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_mmio.c +77 ~~-73~~

150 lines not on this page · raw message

drivers/gpu/drm/xe/xe_mmio.h +59 ~~-17~~

76 lines not on this page · raw message

drivers/gpu/drm/xe/xe_pci.c +11 -0

index da09c26249f5f..9d807d9a0807a 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_reg_sr.c +5 -4

index 52969c0909659..d3773a9853872 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_trace.h +4 -3

index 8573d7a87d840..91130ad8999cd 100644

Lines of this file are not shown. View the raw message.

drivers/gpu/drm/xe/xe_wa.c +31 ~~-25~~

56 lines not on this page · raw message

drivers/gpu/drm/xe/xe_wa_oob.rules +3 -2

index 93fa2708ee378..97d14b2119ecf 100644

Lines of this file are not shown. View the raw message.

drivers/hid/Kconfig +1 -0

index 95a4ede270991..f283f271d87e7 100644

Lines of this file are not shown. View the raw message.

drivers/hid/hid-apple.c +1 -0

index a0f79803df3bd..b0cf13cd292bd 100644

Lines of this file are not shown. View the raw message.

drivers/hid/hid-elecom.c +16 -0

index b57b6deb36f42..f1e3fc374a1d5 100644

Lines of this file are not shown. View the raw message.

drivers/hid/hid-ids.h +4 -0

index 9d0a97a3b06a2..dfa39a37405e3 100644

Lines of this file are not shown. View the raw message.

drivers/hid/hid-logitech-hidpp.c +3 -1

index c470b4f0e9211..492a02ca80594 100644

Lines of this file are not shown. View the raw message.

drivers/hid/hid-magicmouse.c +5 -0

index 542b3e86d56f4..19c811f9ae074 100644

Lines of this file are not shown. View the raw message.

drivers/hid/hid-multitouch.c +3 -0

index fcfc508d1b54d..c3a914458358c 100644

Lines of this file are not shown. View the raw message.

drivers/hid/hid-pl.c +6 -1

index 3c8827081deae..dc11d5322fc0f 100644

Lines of this file are not shown. View the raw message.

drivers/hid/hid-playstation.c +3 -1

index 71a8d4ec9913b..b13a8f27cda0c 100644

Lines of this file are not shown. View the raw message.

drivers/hid/hid-prodikeys.c +4 -0

index 3d08c190a935b..af7366b37c07b 100644

Lines of this file are not shown. View the raw message.

drivers/hid/hid-quirks.c +3 -0

index 1f531626192cd..7a3e0675d9ba2 100644

Lines of this file are not shown. View the raw message.

drivers/hid/i2c-hid/i2c-hid-of-elan.c +8 -0

index 3fcff6daa0d3a..f215bad8b3ab1 100644

Lines of this file are not shown. View the raw message.

drivers/hid/intel-ish-hid/ishtp/bus.c +1 -1

index fddc1c4b6cedb..03c68fe40925b 100644

Lines of this file are not shown. View the raw message.

drivers/hv/vmbus_drv.c +65 -1

66 lines not on this page · raw message

drivers/hwmon/dell-smm-hwmon.c +7 -0

index 9df78861f5f88..2cb92a53e7c2c 100644

Lines of this file are not shown. View the raw message.

drivers/hwmon/f71882fg.c +4 -2

index 7c941d320a186..734df959276af 100644

Lines of this file are not shown. View the raw message.

drivers/hwmon/ibmpex.c +2 -7

index 129f3a9e8fe96..228c5f6c6f383 100644

Lines of this file are not shown. View the raw message.

drivers/hwmon/nct6775-platform.c +1 -0

index 1218a3b449a80..ece183a0d4e91 100644

Lines of this file are not shown. View the raw message.

drivers/hwmon/pmbus/mpq8785.c +103 -8

111 lines not on this page · raw message

drivers/hwspinlock/omap_hwspinlock.c +3 -1

index 27b47b8623c09..2d8de835bc242 100644

Lines of this file are not shown. View the raw message.

drivers/hwtracing/coresight/coresight-etm3x-core.c +6 -6

index c103f4c70f5d0..994ae1e08af8b 100644

Lines of this file are not shown. View the raw message.

drivers/i3c/master.c +4 -2

index 6eb779affaba8..fe6f956cc3111 100644

Lines of this file are not shown. View the raw message.

drivers/i3c/master/dw-i3c-master.c +3 -0

index dbcd3984f2578..4c019c746f231 100644

Lines of this file are not shown. View the raw message.

drivers/i3c/master/mipi-i3c-hci/dma.c +8 -0

index fe955703e59b5..68c2923f55664 100644

Lines of this file are not shown. View the raw message.

drivers/i3c/master/svc-i3c-master.c +2 -2

index 985f30ef0c939..cc13892e45963 100644

Lines of this file are not shown. View the raw message.

drivers/iio/accel/adxl380.c +1 -0

index 10ed3b04ca307..cfd24ef538a64 100644

Lines of this file are not shown. View the raw message.

drivers/iio/accel/bma180.c +3 -2

index 2445a0f7bc2ba..ff64bfb348ed8 100644

Lines of this file are not shown. View the raw message.

drivers/iio/accel/sca3000.c +5 -1

index 87c54e41f6ccd..2b87f7f5508bb 100644

Lines of this file are not shown. View the raw message.

drivers/iio/adc/ad7766.c +1 -1

index 4d570383ef025..1e6bfe8765ab3 100644

Lines of this file are not shown. View the raw message.

drivers/iio/gyro/itg3200_buffer.c +3 -5

index 4cfa0d4395605..d1c125a77308a 100644

Lines of this file are not shown. View the raw message.

drivers/iio/gyro/itg3200_core.c +2 -0

index cd8a2dae56cd9..bfe95ec1abda9 100644

Lines of this file are not shown. View the raw message.

drivers/iio/gyro/mpu3050-core.c +2 -4

index 35af68b41408f..4dcd0cc545518 100644

Lines of this file are not shown. View the raw message.

drivers/iio/light/si1145.c +1 -1

index 66abda021696a..1050bf68e076e 100644

Lines of this file are not shown. View the raw message.

drivers/iio/magnetometer/ak8975.c +1 -1

index 18077fb463a91..6975e0af50536 100644

Lines of this file are not shown. View the raw message.

drivers/iio/pressure/mprls0025pa.c +15 ~~-21~~

index 3b6145348c2e3..e13e6a7ef8db9 100644

Lines of this file are not shown. View the raw message.

drivers/iio/pressure/mprls0025pa.h +0 -2

index d62a018eaff32..b6944b3051267 100644

Lines of this file are not shown. View the raw message.

drivers/iio/pressure/mprls0025pa_spi.c +14 -5

index 3aed14cd95c5a..241ad36f6501a 100644

Lines of this file are not shown. View the raw message.

drivers/iio/test/Kconfig +0 -1

index 33cca49c8058a..3b6d9b1476d8c 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/core/cache.c +15 -1

index a1291f475466d..f513c4fe9f38d 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/core/core_priv.h +3 -0

index 05102769a918a..a2c36666e6fcb 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/core/device.c +33 -1

index bbc131737378e..666ce83cc35c4 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/core/iwcm.c +21 ~~-35~~

56 lines not on this page · raw message

drivers/infiniband/core/iwcm.h +0 -1

index bf74639be1287..b56fb12edece4 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/core/rw.c +38 ~~-15~~

53 lines not on this page · raw message

drivers/infiniband/core/umem_dmabuf.c +1 -3

index 9fcd37761264a..44bb7449738cf 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/core/user_mad.c +6 -2

index fd67fc9fe85a4..2f7e3c4483fc5 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/core/uverbs_cmd.c +5 -2

index 535bb99ed9f5f..ac81b7d1eec96 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/hw/efa/efa_verbs.c +1 -1

index 46eddef7a1cc9..fb6b29972fcce 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/hw/hns/hns_roce_ah.c +11 ~~-12~~

index 307c35888b300..3b6c6a6e9f977 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/hw/hns/hns_roce_hw_v2.c +40 ~~-14~~

54 lines not on this page · raw message

drivers/infiniband/hw/mlx5/main.c +80 ~~-15~~

95 lines not on this page · raw message

drivers/infiniband/hw/mlx5/mlx5_ib.h +2 -0

index f49cb588a856d..3135519f1cfdf 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/hw/mlx5/std_types.c +2 -2

index bdb568411091c..d0137ab7c645c 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/sw/rxe/rxe_comp.c +3 -0

index d48af21807458..e02c5df0bef14 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/sw/rxe/rxe_req.c +3 -0

index 87a02f0deb000..d08ebb048cb0f 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/sw/rxe/rxe_srq.c +3 -3

index 2a234f26ac104..c9a7cd38953d3 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/sw/siw/siw_qp_rx.c +2 -1

index ed4fc39718b49..06738f582c7af 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/ulp/rtrs/rtrs-clt.c +2 -2

index 2b397a544cb93..8fa1d72bd20a4 100644

Lines of this file are not shown. View the raw message.

drivers/infiniband/ulp/rtrs/rtrs-srv.c +21 ~~-12~~

index 9ecc6343455d6..adb798e2a54ae 100644

Lines of this file are not shown. View the raw message.

drivers/interconnect/mediatek/icc-emi.c +6 -3

index 7da740b5fa8d6..dfa3a9cd93998 100644

Lines of this file are not shown. View the raw message.

drivers/iommu/amd/iommu.c +17 -8

index 5fb7bb7a84f41..fecca5c32e8a2 100644

Lines of this file are not shown. View the raw message.

drivers/iommu/arm/arm-smmu-v3/arm-smmu-v3.c +21 ~~-10~~

index 560a670ee7911..5d11e5177a3c9 100644

Lines of this file are not shown. View the raw message.

drivers/iommu/intel/Makefile +1 -1

index c8beb0281559f..d3bb0798092df 100644

Lines of this file are not shown. View the raw message.

drivers/iommu/intel/iommu.c +6 ~~-13~~

index c799cc67db34e..d4f852f712aa8 100644

Lines of this file are not shown. View the raw message.

drivers/iommu/intel/iommu.h +6 -8

index 5b5f57d694afd..b33d8888d7ebd 100644

Lines of this file are not shown. View the raw message.

drivers/iommu/intel/pasid.c +12 -5

index 2e5fa0a232999..90fdfa5f7d1d6 100644

Lines of this file are not shown. View the raw message.

drivers/iommu/intel/pasid.h +14 -0

index dde6d3ba5ae0f..55cad7bfa294e 100644

Lines of this file are not shown. View the raw message.

drivers/iommu/intel/prq.c new file +402 -0

402 lines not on this page · raw message

drivers/iommu/intel/svm.c +0 ~~-397~~

397 lines not on this page · raw message

drivers/leds/rgb/leds-qcom-lpg.c +5 -3

index 84e02867f3b43..98c60e971b48f 100644

Lines of this file are not shown. View the raw message.

drivers/mailbox/bcm-flexrm-mailbox.c +2 ~~-12~~

index b1abc2a0c971a..b616a8eacc0ee 100644

Lines of this file are not shown. View the raw message.

drivers/mailbox/imx-mailbox.c +6 -2

index 0657bd3d8f97b..aa9a299859d6a 100644

Lines of this file are not shown. View the raw message.

drivers/mailbox/pcc.c +1 -1

index 2b7d0bc920726..1d4191cb91380 100644

Lines of this file are not shown. View the raw message.

drivers/mailbox/sprd-mailbox.c +9 ~~-11~~

index ee8539dfcef54..46d0c34177ab9 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm-exception-store.c +1 -1

index c3799757bf4a0..88f119a0a2ae0 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm-integrity.c +14 -1

index 444cf35feebf4..e1dc373ad209d 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm-log.c +1 -1

index 9d85d045f9d9d..bced5a783ee33 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm-mpath.c +1 -1

index 637977acc3dc0..6e68a22f0d283 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm-path-selector.c +1 -1

index 3e4cb81ce512c..78f98545ca72d 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm-rq.c +11 -5

index 499f8cc8a39fb..29d6ee68d4dfb 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm-target.c +1 -1

index b676fd01a0227..33f81611bdefd 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm-unstripe.c +1 -1

index e8a9432057dce..17be483595642 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm-verity-fec.c +2 -2

index 7d477ff6f26bb..6f98065d8e5cc 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm-zone.c +7 -4

index 04cc36a9d5ca4..912b9fe1f5648 100644

Lines of this file are not shown. View the raw message.

drivers/md/dm.c +2 -0

index fd84a126f63fb..ec48fcdb19ed8 100644

Lines of this file are not shown. View the raw message.

drivers/md/md-bitmap.c +2 -1

index e7e1833ff04b2..21cdf48815f88 100644

Lines of this file are not shown. View the raw message.

drivers/md/md-cluster.c +6 -1

index 6595f89becdb7..bf9ab478df2c0 100644

Lines of this file are not shown. View the raw message.

drivers/md/raid1.c +8 -1

index 4c6b1bd6da9bb..093b04e6be675 100644

Lines of this file are not shown. View the raw message.

drivers/md/raid10.c +1 -1

index a91911a9fc036..db07c99c4d947 100644

Lines of this file are not shown. View the raw message.

drivers/md/raid5.c +2 -1

index 7262b77a8e022..5079943046743 100644

Lines of this file are not shown. View the raw message.

drivers/media/dvb-core/dmxdev.c +4 -4

index 9ce5f010de3f8..804fb339f7355 100644

Lines of this file are not shown. View the raw message.

drivers/media/dvb-core/dvb_vb2.c +3 -2

index 29edaaff7a5c9..7444bbc2f24d9 100644

Lines of this file are not shown. View the raw message.

drivers/media/i2c/adv7180.c +7 -0

index f3f47beff76bb..36e0f7a8c6d57 100644

Lines of this file are not shown. View the raw message.

drivers/media/i2c/ccs/ccs-core.c +25 -3

index 4b7d8039b1c9f..9ed35f1227efa 100644

Lines of this file are not shown. View the raw message.

drivers/media/i2c/mt9m114.c +11 -5

index c00f9412d08eb..4100f7ffe5e16 100644

Lines of this file are not shown. View the raw message.

drivers/media/i2c/ov01a10.c +27 ~~-19~~

46 lines not on this page · raw message

drivers/media/i2c/ov5647.c +13 ~~-11~~

index a727beb9d57e2..305677913a0c3 100644

Lines of this file are not shown. View the raw message.

drivers/media/i2c/tw9903.c +1 -0

index b996a05e56f28..c3eafd5d5dc82 100644

Lines of this file are not shown. View the raw message.

drivers/media/i2c/tw9906.c +1 -0

index 6220f4fddbabc..0ab43fe42d7f4 100644

Lines of this file are not shown. View the raw message.

drivers/media/pci/cx23885/cx23885-alsa.c +3 -1

index 25dc8d4dc5b73..717fc6c9ef21f 100644

Lines of this file are not shown. View the raw message.

drivers/media/pci/cx25821/cx25821-alsa.c +1 -0

index a42f0c03a7ca8..f463365163b7e 100644

Lines of this file are not shown. View the raw message.

drivers/media/pci/cx25821/cx25821-core.c +1 -0

index 6627fa9166d30..a7336be444748 100644

Lines of this file are not shown. View the raw message.

drivers/media/pci/cx88/cx88-alsa.c +3 -1

index 29fb1311e4434..4e574d8390b4d 100644

Lines of this file are not shown. View the raw message.

drivers/media/pci/intel/ipu6/ipu6-isys-queue.c +5 -3

index bbb66b56ee88c..c2acf70af347e 100644

Lines of this file are not shown. View the raw message.

drivers/media/pci/intel/ipu6/ipu6-isys-video.c +3 -3

index 48388c0c851ca..f25ea042598b0 100644

Lines of this file are not shown. View the raw message.

drivers/media/pci/intel/ipu6/ipu6-mmu.c +2 -2

index 57298ac73d072..4a46f21f469f0 100644

Lines of this file are not shown. View the raw message.

drivers/media/pci/intel/ipu6/ipu6.c +6 -4

index 1c5c38a30e629..5352219c019c9 100644

Lines of this file are not shown. View the raw message.

drivers/media/pci/mgb4/mgb4_trigger.c +1 -1

index d7dddc5c8728e..10c23f0c833d5 100644

Lines of this file are not shown. View the raw message.

drivers/media/pci/solo6x10/solo6x10-tw28.c +7 -1

index 1b7c22a9bc94f..8f53946c67928 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/amphion/vdec.c +1 -0

index 6a38a0fa0e2d4..86abc1ca202c6 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/amphion/vpu_v4l2.c +0 -2

index 87f5b1d892ca1..72e23f95d6b72 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/chips-media/wave5/wave5-vpu-dec.c +3 -1

index e238447c88bbf..8f7154932d24c 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/chips-media/wave5/wave5-vpu-enc.c +7 -2

index 3e35a05c2d8df..dd34946873ace 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/chips-media/wave5/wave5-vpu.c +6 -4

index b13c5cd46d7e4..4f7eda0504abe 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/mediatek/mdp/mtk_mdp_core.c +15 -2

index 917cdf38f230e..98540015b1cca 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/mediatek/vcodec/decoder/mtk_vcodec_dec_stateless.c +6 -0

index 3307dc15fc1df..f5aa0b06f9e70 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/mediatek/vcodec/encoder/mtk_vcodec_enc.c +3 -3

index 7eaf0e24c9fc4..3cbc4beb2c40f 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/qcom/camss/camss-vfe-480.c +4 -2

index dc2735476c823..003e1900d3c98 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/qcom/venus/vdec.c +10 -4

index 6846973a11594..bc7325a2f197e 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/rockchip/rga/rga-buf.c +3 -0

index 70808049d2e81..ddc244ffc68c1 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/rockchip/rkisp1/rkisp1-params.c +0 -6

index 320581a9f866e..ba6fff91fa17a 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/st/stm32/stm32-dcmipp/dcmipp-bytecap.c +3 -0

index 0f6918f4db383..b461d86bed540 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/ti/omap3isp/isppreview.c +8 ~~-13~~

index e383a57654de8..5c492b31b5160 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/ti/omap3isp/ispvideo.c +11 -3

index daca689dc0825..b9e0b6215fa04 100644

Lines of this file are not shown. View the raw message.

drivers/media/platform/verisilicon/rockchip_vpu981_hw_av1_dec.c +37 -6

43 lines not on this page · raw message

drivers/media/radio/radio-keene.c +1 -1

index a35648316aa8d..05d3c4b567211 100644

Lines of this file are not shown. View the raw message.

drivers/media/usb/pvrusb2/pvrusb2-hdw.c +5 -0

index 2de104736f874..943d56b10251b 100644

Lines of this file are not shown. View the raw message.

drivers/media/usb/uvc/uvc_video.c +2 -1

index 57e6f9af536ff..57bccbf17f6dc 100644

Lines of this file are not shown. View the raw message.

drivers/media/v4l2-core/v4l2-async.c +31 ~~-14~~

45 lines not on this page · raw message

drivers/mfd/Kconfig +24 -0

index f9325bcce1b94..f08b8009eeea0 100644

Lines of this file are not shown. View the raw message.

drivers/mfd/arizona-core.c +1 -1

index 85ff8717d8504..91975536d14d2 100644

Lines of this file are not shown. View the raw message.

drivers/mfd/da9052-spi.c +1 -1

index 80fc5c0cac2fb..be5f2b34e18ae 100644

Lines of this file are not shown. View the raw message.

drivers/mfd/intel-lpss-pci.c +13 -0

index 5b1c13fb23468..a7feb82c28e3f 100644

Lines of this file are not shown. View the raw message.

drivers/mfd/mfd-core.c +22 ~~-14~~

index 7d14a1e7631ee..c55223ce4327a 100644

Lines of this file are not shown. View the raw message.

drivers/mfd/omap-usb-host.c +4 -2

index 6de7ba7523455..e25957c808124 100644

Lines of this file are not shown. View the raw message.

drivers/mfd/qcom-pm8xxx.c +1 -7

index 8b6285f687da5..0e490591177a2 100644

Lines of this file are not shown. View the raw message.

drivers/mfd/simple-mfd-i2c.c +32 -1

index 6eda79533208a..908eae338fee0 100644

Lines of this file are not shown. View the raw message.

drivers/misc/bcm-vk/bcm_vk_msg.c +8 -4

index 1f42d1d5a630a..665a3888708ac 100644

Lines of this file are not shown. View the raw message.

drivers/misc/eeprom/eeprom_93xx46.c +3 -8

index e2221be884458..cc7599f08b391 100644

Lines of this file are not shown. View the raw message.

drivers/most/core.c +12 -3

index da319d108ea1d..40d63e38fef54 100644

Lines of this file are not shown. View the raw message.

drivers/mtd/nand/raw/cadence-nand-controller.c +1 -1

index 443202b942e1f..5872f1dfe7016 100644

Lines of this file are not shown. View the raw message.

drivers/mtd/nand/raw/pl35x-nand-controller.c +1 -0

index 2570fd0beea0d..13c187af5a86f 100644

Lines of this file are not shown. View the raw message.

drivers/mtd/nand/spi/core.c +8 -0

index 57b8807b19482..48ac009cbaad2 100644

Lines of this file are not shown. View the raw message.

drivers/mtd/parsers/ofpart_core.c +14 -2

index abfa687989182..09961c6f39496 100644

Lines of this file are not shown. View the raw message.

drivers/mtd/parsers/tplink_safeloader.c +1 -0

index e358a029dc70c..4fcaf92d22e4f 100644

Lines of this file are not shown. View the raw message.

drivers/net/bonding/bond_main.c +14 -7

index 209cab75ac0a5..dd1f8cad953bf 100644

Lines of this file are not shown. View the raw message.

drivers/net/caif/caif_serial.c +3 -2

index ed3a589def6b1..699ed0ff461e8 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/broadcom/bnxt/bnxt.c +7 -6

index 8799db6f3c866..7b84ed5c300e6 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/broadcom/bnxt/bnxt_ethtool.c +7 -6

index 54ae90526d8ff..0a8f3dc3c2f01 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/cadence/macb_main.c +5 -6

index 095c1cfcc9a1d..f258c4b82c74d 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/ec_bhf.c +1 -1

index 44af1d13d9317..4f1d7d216b5e3 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/freescale/dpaa2/dpaa2-switch.c +7 -0

index 6ea58fc22783f..e78f400784770 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/hisilicon/hns3/hns3_enet.c +9 -2

index b477bd286ed72..803da392c8efe 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/hisilicon/hns3/hns3pf/hclge_cmd.h +3 -2

index 416e02e7b995f..bc333d8710ac1 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/hisilicon/hns3/hns3pf/hclge_main.c +3 -1

index 7468e03051ea4..434f40ce3062b 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/intel/i40e/i40e_main.c +7 -1

index 2dc737c7e3fd8..31c83fc69cf41 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeon_ep/octep_cn9k_pf.c +17 -4

index b5805969404fa..01e82d0b6b2cd 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeon_ep/octep_cnxk_pf.c +53 ~~-11~~

64 lines not on this page · raw message

drivers/net/ethernet/marvell/octeon_ep/octep_main.h +1 -1

index 936b786f42816..c063c8451d47a 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeon_ep/octep_regs_cn9k_pf.h +1 -0

index ca473502d7a02..95f1dfff90cce 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeon_ep/octep_regs_cnxk_pf.h +1 -0

index e637d7c8224d4..4d172a552f80c 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeon_ep/octep_rx.c +7 -1

index 82b6b19e76b47..f2a7c6a76c742 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeon_ep_vf/octep_vf_cn9k.c +2 -1

index 88937fce75f14..4c769b27c2789 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeon_ep_vf/octep_vf_cnxk.c +36 -3

index 1f79dfad42c62..a968b93a67943 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeon_ep_vf/octep_vf_main.h +1 -1

index 1a352f41f823c..4ee6b4d568ede 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeon_ep_vf/octep_vf_rx.c +7 -1

index d70c8be3cfc40..6f865dbbba6c6 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeontx2/af/cgx.c +2 -0

index ca74bf6843369..394061a3d38c7 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeontx2/af/rvu.c +11 -0

index 74201e0210bbf..d5e2ebedd433e 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeontx2/af/rvu_nix.c +9 -3

index da69350c6f765..0a23e0a918280 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/octeontx2/af/rvu_npc.c +22 ~~-19~~

41 lines not on this page · raw message

drivers/net/ethernet/marvell/octeontx2/nic/otx2_pf.c +1 -0

index 5492dea547a19..2de9c44ef57c7 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/marvell/skge.c +0 -1

index fcfb34561882b..7d398c16ea720 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/mellanox/mlx5/core/en.h +2 -1

index 8245a149cdf85..0e18906168313 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/mellanox/mlx5/core/en_accel/ipsec.c +96 ~~-17~~

113 lines not on this page · raw message

drivers/net/ethernet/mellanox/mlx5/core/en_accel/ipsec.h +9 ~~-17~~

index 78e78b6f81467..a37c8a117d80f 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/mellanox/mlx5/core/en_accel/ipsec_fs.c +42 ~~-33~~

75 lines not on this page · raw message

drivers/net/ethernet/mellanox/mlx5/core/eswitch_offloads.c +2 -0

index f4cb3e78d0651..7cead1ba0bfa1 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/mellanox/mlx5/core/sriov.c +2 -0

index a2fc937d54617..172862a70c70d 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/mellanox/mlx5/core/steering/dr_dbg.c +2 -2

index 030a5776c9374..a4c19af1775f1 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/microchip/sparx5/sparx5_ptp.c +1 -1

index 5a932460db581..6b2dbfbeef377 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/microchip/sparx5/sparx5_qos.h +1 -1

index ced35033a6c5d..b1c6c5c6f16ca 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/mscc/ocelot_net.c +56 ~~-19~~

75 lines not on this page · raw message

drivers/net/ethernet/myricom/myri10ge/myri10ge.c +27 -1

index b7d9657a7af3d..3f2086873a483 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/pensando/ionic/ionic_ethtool.c +4 -3

index 9b7f78b6cdb1e..a632536bd7f2f 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/sun/sunhme.c +3 -0

index 50ace461a1af4..89ac15190770d 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/ti/Kconfig +1 -0

index 3a13d60a947a8..cd0a196e6ee3d 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/ti/cpsw_new.c +5 -7

index 0eee1a0527b5c..a74caaca94d11 100644

Lines of this file are not shown. View the raw message.

drivers/net/ethernet/xscale/ixp4xx_eth.c +27 ~~-33~~

60 lines not on this page · raw message

drivers/net/ethernet/xscale/ptp_ixp46x.c +3 -0

index 94203eb46e6b0..93c64db22a696 100644

Lines of this file are not shown. View the raw message.

drivers/net/macvlan.c +5 -0

index aaf7d755fc8a1..3770bc84a9445 100644

Lines of this file are not shown. View the raw message.

drivers/net/mctp/mctp-i2c.c +9 -0

index 503a9174321c6..617333343ca00 100644

Lines of this file are not shown. View the raw message.

drivers/net/phy/sfp.c +6 -2

index 6153a35af1070..cae748b762236 100644

Lines of this file are not shown. View the raw message.

drivers/net/usb/Kconfig +0 -1

index 3c360d4f06352..73498a3ea44ce 100644

Lines of this file are not shown. View the raw message.

drivers/net/usb/catc.c +31 -6

index ff439ef535ac9..98346cb4ece01 100644

Lines of this file are not shown. View the raw message.

drivers/net/usb/kaweth.c +0 -2

index c9efb7df892ec..e01d14f6c3667 100644

Lines of this file are not shown. View the raw message.

drivers/net/usb/lan78xx.c +0 -2

index 2da67814556f9..4bb53919a1d7e 100644

Lines of this file are not shown. View the raw message.

drivers/net/usb/pegasus.c +30 -5

index c514483134f05..0f16a133c75d1 100644

Lines of this file are not shown. View the raw message.

drivers/net/usb/r8152.c +2 -0

index d27e62939bf13..e4eb4e5425364 100644

Lines of this file are not shown. View the raw message.

drivers/net/usb/sr9700.c +4 ~~-21~~

index 213b4817cfdf6..e4d7bcd0d99c2 100644

Lines of this file are not shown. View the raw message.

drivers/net/usb/sr9700.h +1 -6

index ea2b4de621c86..c479908f7d823 100644

Lines of this file are not shown. View the raw message.

drivers/net/wan/farsync.c +2 -0

index 5b01642ca44e0..6b2d1e63855e8 100644

Lines of this file are not shown. View the raw message.

drivers/net/wan/fsl_ucc_hdlc.c +2 -6

index 605e70f7baace..675f4b0eb502f 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/ath/ath10k/sdio.c +6 -0

index 6805357ee29e6..2ff2dc4a3f58b 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/ath/ath10k/wmi.c +2 -2

index fef7d9b081963..408f062a4306f 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/ath/ath11k/core.c +28 -0

index 735032c353b2d..c6d17dbbdb376 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/ath/ath11k/reg.c +6 -3

index d62a2014315a0..49b79648752cf 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/ath/ath12k/wmi.c +1 -1

index 5c5fc2b7642f6..761c169c992f1 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/intel/ipw2x00/ipw2200.c +7 -1

index eed9ef17bc293..38d6d5617cce5 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/intel/iwlegacy/3945-mac.c +2 -0

index 74fc76c00ebcf..20d2afe1d55f9 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/intel/iwlegacy/4965-mac.c +2 -0

index a94cf27ffe4b0..ac2cfef737e4f 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/intel/iwlwifi/mvm/mac-ctxt.c +14 -0

index d013de30e7ed6..28d329ec31b82 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/marvell/libertas/if_usb.c +2 -0

index 2240b4db8c036..d98c81539ba53 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw88/main.c +32 ~~-15~~

47 lines not on this page · raw message

drivers/net/wireless/realtek/rtw88/main.h +1 -1

index c808bb271e9d0..b70b6e62449cc 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw88/rtw8821cu.c +2 -0

index a019f4085e738..1f5af09aed99f 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw88/rtw8822b.c +2 -1

index 4a6c0a9266a09..0dba4b4c9464e 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw89/fw.c +3 -0

index ae2c4ff74531a..b62b59bf528e7 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw89/mac.c +1 -0

index b956ea2add919..31465893f866d 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw89/mac.h +1 -0

index 7974849f41e25..ad496a4f441aa 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw89/mac_be.c +2 -1

index f22eaa83297fb..2896abce94a3c 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw89/pci.c +1 -0

index a87e1778a0d41..c3a8a7af06472 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw89/rtw8922a.c +65 ~~-14~~

79 lines not on this page · raw message

drivers/net/wireless/realtek/rtw89/ser.c +10 -0

index 2a303a758e276..43970d0e5b33f 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw89/wow.c +4 -0

index fdb715dc175c1..db68ac988cd24 100644

Lines of this file are not shown. View the raw message.

drivers/net/wireless/realtek/rtw89/wow.h +1 -0

index f91991e8f2e30..d4b618fa4e3e5 100644

Lines of this file are not shown. View the raw message.

drivers/net/wwan/mhi_wwan_mbim.c +2 -1

index f8bc9a39bfa30..1d7e3ad900c12 100644

Lines of this file are not shown. View the raw message.

drivers/net/xen-netback/xenbus.c +3 -2

index a78a25b872409..61b547aab286a 100644

Lines of this file are not shown. View the raw message.

drivers/nfc/nxp-nci/i2c.c +1 -1

index 049662ffdf972..6a5ce8ff91f0b 100644

Lines of this file are not shown. View the raw message.

drivers/ntb/hw/mscc/ntb_hw_switchtec.c +10 -2

index f851397b65d6e..0536521fa6ccc 100644

Lines of this file are not shown. View the raw message.

drivers/ntb/ntb_transport.c +2 -2

index 4f775c3e218f4..868a2baef1d52 100644

Lines of this file are not shown. View the raw message.

drivers/nvdimm/nd_virtio.c +2 -1

index f55d60922b87d..e8ac7425c97cd 100644

Lines of this file are not shown. View the raw message.

drivers/nvdimm/virtio_pmem.c +1 -0

index c9b97aeabf854..89d3d4fc3ce89 100644

Lines of this file are not shown. View the raw message.

drivers/nvdimm/virtio_pmem.h +4 -0

index 0dddefe594c46..f72cf17f9518f 100644

Lines of this file are not shown. View the raw message.

drivers/nvmem/core.c +1 -0

index d1869e6de3844..021bf3310fb2a 100644

Lines of this file are not shown. View the raw message.

drivers/of/unittest.c +4 -2

index 63b5b435bd3ae..ba223736237e8 100644

Lines of this file are not shown. View the raw message.

drivers/opp/core.c +1 -1

index 5ac209472c0cf..b5df41ce3afff 100644

Lines of this file are not shown. View the raw message.

drivers/pci/controller/dwc/pcie-designware-host.c +8 -1

index d428457d9c432..3e3168204e303 100644

Lines of this file are not shown. View the raw message.

drivers/pci/controller/dwc/pcie-qcom.c +1 -3

index 2fca35dd72a76..5d27cd149f512 100644

Lines of this file are not shown. View the raw message.

drivers/pci/controller/pcie-mediatek.c +3 -1

index 7f7d04c2ea573..c4cc9d76b42a0 100644

Lines of this file are not shown. View the raw message.

drivers/pci/endpoint/pci-ep-cfs.c +4 -4

index 43feb6139fa36..8b392a8363bb1 100644

Lines of this file are not shown. View the raw message.

drivers/pci/iov.c +4 -5

index 44a33df3c69c2..d595a345a7d47 100644

Lines of this file are not shown. View the raw message.

drivers/pci/msi/msi.c +3 -1

index 8b88487886184..54627c3a2dc8c 100644

Lines of this file are not shown. View the raw message.

drivers/pci/p2pdma.c +1 -0

index 52e1564eadd0b..ec53b2b0d57fe 100644

Lines of this file are not shown. View the raw message.

drivers/pci/pci-acpi.c +24 ~~-35~~

59 lines not on this page · raw message

drivers/pci/pci-driver.c +8 -0

index a00a2ce01045f..9846ab70cff11 100644

Lines of this file are not shown. View the raw message.

drivers/pci/pci.c +23 ~~-19~~

42 lines not on this page · raw message

drivers/pci/pci.h +8 -0

index c951f861a69b2..b9b97ec0f836a 100644

Lines of this file are not shown. View the raw message.

drivers/pci/pcie/aer.c +25 -4

index e5cbea3a4968b..fe7603e7ee8c8 100644

Lines of this file are not shown. View the raw message.

drivers/pci/pcie/portdrv.c +3 -3

index ec2c768c687f0..75068c5029b01 100644

Lines of this file are not shown. View the raw message.

drivers/pci/probe.c +41 -4

45 lines not on this page · raw message

drivers/pci/quirks.c +27 -0

index 18fa918b4e537..3d05ea35c536f 100644

Lines of this file are not shown. View the raw message.

drivers/perf/arm-cmn.c +18 -1

index e6b0c8ec9c1fa..9a20008ad4a1e 100644

Lines of this file are not shown. View the raw message.

drivers/perf/arm_spe_pmu.c +12 -6

index abd23430dc033..2fce871a1882d 100644

Lines of this file are not shown. View the raw message.

drivers/perf/cxl_pmu.c +1 -1

index 16328569fde93..24244096f5141 100644

Lines of this file are not shown. View the raw message.

drivers/phy/cadence/phy-cadence-torrent.c +23 -0

index 8bbbbb87bb22e..92feb45fb56e6 100644

Lines of this file are not shown. View the raw message.

drivers/phy/freescale/phy-fsl-imx8mq-usb.c +1 -0

index 043063699e064..41194083e358c 100644

Lines of this file are not shown. View the raw message.

drivers/phy/freescale/phy-fsl-imx8qm-hsio.c +1 -1

index 977d21d753a59..279b8ac7822df 100644

Lines of this file are not shown. View the raw message.

drivers/phy/marvell/phy-mvebu-cp110-utmi.c +1 -1

index 4922a5f3327d5..30391d0d7d4b4 100644

Lines of this file are not shown. View the raw message.

drivers/phy/qualcomm/phy-qcom-edp.c +8 -8

index da2b32fb5b451..dddb06a1afe49 100644

Lines of this file are not shown. View the raw message.

drivers/phy/ti/phy-j721e-wiz.c +17 -2

index c6e846d385d28..cbcc7bd5dde0a 100644

Lines of this file are not shown. View the raw message.

drivers/pinctrl/intel/Kconfig +15 -6

index 14c26c023590e..75e19a062c185 100644

Lines of this file are not shown. View the raw message.

drivers/pinctrl/pinctrl-equilibrium.c +1 -0

index 3a9a0f059090f..c82491da2cc9f 100644

Lines of this file are not shown. View the raw message.

drivers/pinctrl/pinctrl-single.c +2 -0

index 2218d65a7d842..a2fb549307adb 100644

Lines of this file are not shown. View the raw message.

drivers/pinctrl/qcom/pinctrl-sm8250-lpass-lpi.c +1 -1

index 9791d9ba5087c..4e90b29640ff0 100644

Lines of this file are not shown. View the raw message.

drivers/platform/chrome/cros_ec_lightbar.c +1 -1

index 1e69f61115a4d..de64292faa24e 100644

Lines of this file are not shown. View the raw message.

drivers/platform/chrome/cros_typec_switch.c +3 -3

index 07a19386dc4ee..b50e4651c6470 100644

Lines of this file are not shown. View the raw message.

drivers/platform/x86/amd/pmf/core.c +61 -1

62 lines not on this page · raw message

drivers/platform/x86/amd/pmf/pmf.h +10 -0

index 34ba0309a33a2..b857ef4498903 100644

Lines of this file are not shown. View the raw message.

drivers/platform/x86/amd/pmf/tee-if.c +3 -9

index a9b195ec6f33f..6254423d05b06 100644

Lines of this file are not shown. View the raw message.

drivers/platform/x86/intel/int0002_vgpio.c +2 -2

index 0171be8867fce..c5c70319b0f37 100644

Lines of this file are not shown. View the raw message.

drivers/platform/x86/intel/speed_select_if/isst_tpmi_core.c +3 -0

index 4045823071091..6c471a0ea6b2d 100644

Lines of this file are not shown. View the raw message.

drivers/power/reset/nvmem-reboot-mode.c +13 -2

index 41530b70cfc48..d260715fccf67 100644

Lines of this file are not shown. View the raw message.

drivers/power/sequencing/core.c +4 -2

index 0ffc259c6bb6c..70b92e1c3ac5e 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/ab8500_charger.c +20 ~~-20~~

index 93181ebfb3247..5da3b12d9f0bb 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/act8945a_charger.c +8 -8

index 51122bfbf196c..699030bfa296a 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/bq256xx_charger.c +6 -6

index 5514d1896bb84..b47b73ed642e5 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/bq25980_charger.c +6 -6

index 0c5e2938bb36d..b3060df9449eb 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/bq27xxx_battery.c +3 -3

index 14be797e89c3d..a5a3ab4f8a631 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/cpcap-battery.c +4 -4

index 30ec76cdf34b0..eaad9f53bb5cc 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/goldfish_battery.c +6 -6

index 479195e35d734..5aa24e4dc4455 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/pm8916_bms_vm.c +9 -9

index 5d0dd842509c4..9b069af077be5 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/pm8916_lbc.c +9 -9

index 6d92e98cbecc6..e6c44f342eeb4 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/qcom_battmgr.c +2 -1

index f8bea732ba7f2..a6576248e761e 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/rt9455_charger.c +9 -8

index 64a23e3d7bb00..803f4d258da9e 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/sbs-battery.c +18 ~~-18~~

index a6c204c08232a..f80edceafc3cf 100644

Lines of this file are not shown. View the raw message.

drivers/power/supply/wm97xx_battery.c +19 ~~-15~~

index 1cc38d1437d91..181bb7ab64d60 100644

Lines of this file are not shown. View the raw message.

drivers/powercap/intel_rapl_msr.c +1 -0

index cbe07450de933..458a90a6d57c0 100644

Lines of this file are not shown. View the raw message.

drivers/powercap/intel_rapl_tpmi.c +1 -1

index 645fd1dc51a98..1618138c5cac1 100644

Lines of this file are not shown. View the raw message.

drivers/rapidio/rio-scan.c +2 -1

index c12941f71e2cb..dcd6619a4b027 100644

Lines of this file are not shown. View the raw message.

drivers/ras/ras.c +5 -1

index c1b36a5601c4b..ae993db1f9c16 100644

Lines of this file are not shown. View the raw message.

drivers/regulator/core.c +30 ~~-25~~

55 lines not on this page · raw message

drivers/remoteproc/imx_dsp_rproc.c +9 -0

index 376187ad5754c..713a57200cf09 100644

Lines of this file are not shown. View the raw message.

drivers/remoteproc/imx_rproc.c +4 -0

index cc3f5b7fe9dd1..2797b7e971429 100644

Lines of this file are not shown. View the raw message.

drivers/remoteproc/mtk_scp.c +28 ~~-11~~

index f98a11d4cf292..ae20d2221c8e0 100644

Lines of this file are not shown. View the raw message.

drivers/remoteproc/mtk_scp_ipi.c +2 -2

index c068227e251e7..7a37e273b3af8 100644

Lines of this file are not shown. View the raw message.

drivers/reset/reset-gpio.c +1 -0

index 2290b25b67035..15353ba5758c3 100644

Lines of this file are not shown. View the raw message.

drivers/rpmsg/rpmsg_core.c +27 ~~-39~~

66 lines not on this page · raw message

drivers/rtc/interface.c +1 -1

index 39db12f267cc6..ee185710262ac 100644

Lines of this file are not shown. View the raw message.

drivers/rtc/rtc-zynqmp.c +3 -0

index b6f96c10196ae..f49af7d963fbd 100644

Lines of this file are not shown. View the raw message.

drivers/s390/cio/css.c +1 -1

index 7b59d20bf7850..61be7c0550bc4 100644

Lines of this file are not shown. View the raw message.

drivers/scsi/BusLogic.c +4 -2

index 2135a2b3e2d00..c17b09d966f14 100644

Lines of this file are not shown. View the raw message.

drivers/scsi/csiostor/csio_scsi.c +2 -1

index 8329f0cab4e7d..b0467251cece0 100644

Lines of this file are not shown. View the raw message.

drivers/scsi/elx/efct/efct_driver.c +1 -7

index 55d2301bfd7de..d1a73cc2398ec 100644

Lines of this file are not shown. View the raw message.

drivers/scsi/smartpqi/smartpqi_init.c +10 -3

index f0fb22e4117eb..e7836f66c89ad 100644

Lines of this file are not shown. View the raw message.

drivers/soc/mediatek/mtk-svs.c +2 -3

index 4cb8169aec6b5..07ab261e1269d 100644

Lines of this file are not shown. View the raw message.

drivers/soc/qcom/cmd-db.c +4 -3

index ae66c2623d250..84a75d8c4b702 100644

Lines of this file are not shown. View the raw message.

drivers/soc/qcom/smem.c +3 -1

index 170f88ce0e50e..493e218c5fd4e 100644

Lines of this file are not shown. View the raw message.

drivers/soc/rockchip/grf.c +28 ~~-29~~

57 lines not on this page · raw message

drivers/soc/ti/k3-socinfo.c +1 -1

index 704039eb3c078..b4e1abd544d14 100644

Lines of this file are not shown. View the raw message.

drivers/soc/ti/pruss.c +2 -4

index 038576805bfa0..0fd59c73f585d 100644

Lines of this file are not shown. View the raw message.

drivers/soundwire/Kconfig +1 -0

index 4d8f3b7024ae5..a057c64d93f0b 100644

Lines of this file are not shown. View the raw message.

drivers/soundwire/dmi-quirks.c +11 -0

index 91ab97a456fa9..5854218e1a274 100644

Lines of this file are not shown. View the raw message.

drivers/soundwire/intel_auxdevice.c +1 -0

index ae689d5d1ab9e..61f07d2d75efc 100644

Lines of this file are not shown. View the raw message.

drivers/spi/spi-geni-qcom.c +20 ~~-18~~

index 768d7482102ad..38606c9e12ee8 100644

Lines of this file are not shown. View the raw message.

drivers/spi/spi-mem.c +23 -3

index 96374afd0193c..ff9f2e9abe619 100644

Lines of this file are not shown. View the raw message.

drivers/spi/spi-stm32.c +5 -4

index 3b1b810f33bf7..e749ce27267fd 100644

Lines of this file are not shown. View the raw message.

drivers/spi/spi-wpcm-fiu.c +1 -1

index a9aee2a6c7dcb..c47b56f0933f1 100644

Lines of this file are not shown. View the raw message.

drivers/spi/spidev.c +22 ~~-41~~

63 lines not on this page · raw message

drivers/staging/greybus/light.c +6 -2

index e509fdc715dbb..38c233a706c48 100644

Lines of this file are not shown. View the raw message.

drivers/staging/rtl8723bs/core/rtw_mlme.c +4 -2

index cbdb134278d37..1f5a23f13dde5 100644

Lines of this file are not shown. View the raw message.

drivers/staging/rtl8723bs/os_dep/ioctl_cfg80211.c +2 -1

index b63a74e669bcf..b300d52e241b5 100644

Lines of this file are not shown. View the raw message.

drivers/staging/rtl8723bs/os_dep/sdio_intf.c +2 -1

index d18fde4e5d6ce..d64998be6b2bb 100644

Lines of this file are not shown. View the raw message.

drivers/thermal/intel/int340x_thermal/processor_thermal_rfim.c +4 -1

index 0e2dc1426282d..c9c7451c34d7e 100644

Lines of this file are not shown. View the raw message.

drivers/thermal/intel/x86_pkg_temp_thermal.c +3 -0

index 8c44f378b61ef..29af9510a6161 100644

Lines of this file are not shown. View the raw message.

drivers/thermal/thermal_of.c +2 -2

index e0aa9d9d5604b..3e674f2d66316 100644

Lines of this file are not shown. View the raw message.

drivers/tty/serial/8250/8250_dw.c +9 -2

index 83d186c038cd9..f17dc3de020c1 100644

Lines of this file are not shown. View the raw message.

drivers/tty/serial/8250/8250_omap.c +22 -3

index 4f57991944dc4..0f4ce0c691147 100644

Lines of this file are not shown. View the raw message.

drivers/tty/serial/Kconfig +4 -4

index 4fd789a77a13b..1e92b16b6b95e 100644

Lines of this file are not shown. View the raw message.

drivers/ufs/core/ufshcd.c +2 -0

index fb406e926d0cc..ba0cc2a051ff3 100644

Lines of this file are not shown. View the raw message.

drivers/ufs/host/Kconfig +1 -0

index 580c8d0bd8bbd..626bb9002f4a1 100644

Lines of this file are not shown. View the raw message.

drivers/ufs/host/ufs-mediatek-trace.h +3 -3

index b5f2ec3140748..0df8ac843379a 100644

Lines of this file are not shown. View the raw message.

drivers/ufs/host/ufs-mediatek.c +3 -9

index 1fb98af4ac564..e4156238f51d9 100644

Lines of this file are not shown. View the raw message.

drivers/usb/chipidea/udc.c +7 -0

index 8f73bd5057a64..5f28aac85d7d4 100644

Lines of this file are not shown. View the raw message.

drivers/usb/dwc2/core.c +1 -0

index 9919ab725d544..368da20ae14d1 100644

Lines of this file are not shown. View the raw message.

drivers/usb/dwc3/core.c +18 -1

index b37a86f2bcca9..526b6a1fa3540 100644

Lines of this file are not shown. View the raw message.

drivers/usb/dwc3/core.h +4 -0

index d47ea3b3528ec..eb8b8f3e52167 100644

Lines of this file are not shown. View the raw message.

drivers/usb/dwc3/gadget.c +3 -5

index 6d1072d041f76..b91093110e688 100644

Lines of this file are not shown. View the raw message.

drivers/usb/gadget/function/f_fs.c +9 ~~-15~~

index f7be1548cc18a..e03ac64361cc5 100644

Lines of this file are not shown. View the raw message.

drivers/usb/gadget/udc/bdc/bdc_core.c +2 -2

index 5149e2b7f0508..7fded329076cc 100644

Lines of this file are not shown. View the raw message.

drivers/usb/gadget/udc/tegra-xudc.c +9 -3

index 3a14b6b72d8c6..114a80dd06fbb 100644

Lines of this file are not shown. View the raw message.

drivers/usb/typec/ucsi/psy.c +20 ~~-10~~

index 7f176382b1a0f..c7d2fb611be4c 100644

Lines of this file are not shown. View the raw message.

drivers/vdpa/mlx5/net/mlx5_vnet.c +0 -3

index 51b2485e874f4..6b8e9da15ed0b 100644

Lines of this file are not shown. View the raw message.

drivers/vdpa/vdpa_sim/vdpa_sim.c +0 -6

index 8ffea8430f95f..481c52be50231 100644

Lines of this file are not shown. View the raw message.

drivers/vfio/pci/hisilicon/hisi_acc_vfio_pci.c +1 -2

index dda8cb3262e0b..1a36b687e0085 100644

Lines of this file are not shown. View the raw message.

drivers/vfio/pci/vfio_pci_core.c +13 -4

index c7ea0b23924af..5f545b45078f8 100644

Lines of this file are not shown. View the raw message.

drivers/vhost/vdpa.c +2 -1

index 5a49b5a6d4964..0ba5237980bbf 100644

Lines of this file are not shown. View the raw message.

drivers/video/backlight/qcom-wled.c +40 -2

42 lines not on this page · raw message

drivers/video/fbdev/au1200fb.c +4 -2

index ed770222660b5..685e629e7e164 100644

Lines of this file are not shown. View the raw message.

drivers/video/fbdev/core/fbcon.c +2 -1

index e681066736dea..abe9e0ad9b43b 100644

Lines of this file are not shown. View the raw message.

drivers/video/fbdev/core/fbcon.h +0 -1

index 4d97e6d8a16a2..7e21c8b336692 100644

Lines of this file are not shown. View the raw message.

drivers/video/fbdev/ffb.c +13 -1

index 34b6abff9493e..da531b4cb4513 100644

Lines of this file are not shown. View the raw message.

drivers/video/fbdev/vt8500lcdfb.c +4 -1

index b08a6fdc53fd2..85c7a99a7d648 100644

Lines of this file are not shown. View the raw message.

drivers/video/of_display_timing.c +5 -5

index bebd371c6b93e..a6ec392253c3e 100644

Lines of this file are not shown. View the raw message.

drivers/watchdog/imx7ulp_wdt.c +1 -0

index 0f13a30533574..03479110453ce 100644

Lines of this file are not shown. View the raw message.

drivers/watchdog/it87_wdt.c +12 -0

index 1a5a0a2c3f2e3..8c42cb41fa230 100644

Lines of this file are not shown. View the raw message.

drivers/watchdog/starfive-wdt.c +1 -1

index 763b11b6f402c..8244f282bee86 100644

Lines of this file are not shown. View the raw message.

drivers/xen/balloon.c +15 -4

index e47bb157aa090..88511187458a9 100644

Lines of this file are not shown. View the raw message.

drivers/xen/grant-dma-ops.c +2 -1

index 29257d2639dbf..43a918c498c6c 100644

Lines of this file are not shown. View the raw message.

drivers/xen/unpopulated-alloc.c +3 -0

index a39f2d36dd9cf..ae46291e99a9d 100644

Lines of this file are not shown. View the raw message.

drivers/xen/xenbus/xenbus_probe_frontend.c +1 -3

index fcb335bb7b187..1fdf5be193430 100644

Lines of this file are not shown. View the raw message.

fs/btrfs/block-rsv.c +4 -3

index a07b9594dc706..a578bd3b32bb0 100644

Lines of this file are not shown. View the raw message.

fs/btrfs/direct-io.c +12 -0

index 71984d7db839b..fb414643f223d 100644

Lines of this file are not shown. View the raw message.

fs/btrfs/extent-tree.c +12 -1

index 7bab2512468d5..c052c8df05fb4 100644

Lines of this file are not shown. View the raw message.

fs/btrfs/qgroup.c +10 -5

index 029017afaf344..71ccba22752cb 100644

Lines of this file are not shown. View the raw message.

fs/btrfs/transaction.c +1 -8

index 7371a3c0bdede..0ee6b40af65ee 100644

Lines of this file are not shown. View the raw message.

fs/btrfs/volumes.c +8 -2

index 9c6e96f630132..24b6a7f83f935 100644

Lines of this file are not shown. View the raw message.

fs/buffer.c +4 -0

index 79c19ffa44015..c5aaf1419d341 100644

Lines of this file are not shown. View the raw message.

fs/ceph/addr.c +22 -2

index 6828a2cff02c8..5addf09cb6e6e 100644

Lines of this file are not shown. View the raw message.

fs/ceph/file.c +16 -1

index 147126d2fa0c7..9e3122db3d780 100644

Lines of this file are not shown. View the raw message.

fs/dlm/lock.c +2 -1

index 0ad496ceb638d..195e4ce22a824 100644

Lines of this file are not shown. View the raw message.

fs/erofs/fileio.c +9 ~~-13~~

index 990defcf93043..2c7f066daacdd 100644

Lines of this file are not shown. View the raw message.

fs/erofs/fscache.c +2 -2

index ce3d8737df85d..20e2cb18ed1d4 100644

Lines of this file are not shown. View the raw message.

fs/ext4/extents.c +52 ~~-13~~

65 lines not on this page · raw message

fs/ext4/ioctl.c +3 -0

index 1c77400bd88e1..99d185d00f377 100644

Lines of this file are not shown. View the raw message.

fs/ext4/mballoc-test.c +1 -1

index f13db95284d9e..8eacba6e780ad 100644

Lines of this file are not shown. View the raw message.

fs/ext4/mballoc.c +16 ~~-28~~

44 lines not on this page · raw message

fs/ext4/super.c +5 -5

index d26a754bb9c83..9eec13f88d5a5 100644

Lines of this file are not shown. View the raw message.

fs/fat/namei_msdos.c +6 -1

index f06f6ba643cc8..c75e3791514a2 100644

Lines of this file are not shown. View the raw message.

fs/fat/namei_vfat.c +6 -1

index 15bf32c21ac0d..31d37e2b4f679 100644

Lines of this file are not shown. View the raw message.

fs/fs_struct.c +1 -0

index 64c2d0814ed68..100bd3474476b 100644

Lines of this file are not shown. View the raw message.

fs/gfs2/bmap.c +12 -1

index 28ad07b003484..776090fbc9aa5 100644

Lines of this file are not shown. View the raw message.

fs/gfs2/glock.c +27 -9

index 54d0eee24e10b..1a1cd631b5880 100644

Lines of this file are not shown. View the raw message.

fs/gfs2/glock.h +2 -1

index 63e101d448e96..b54cc21cac7e6 100644

Lines of this file are not shown. View the raw message.

fs/gfs2/inode.c +30 -4

index 90c7a795112d6..c37079718fdd5 100644

Lines of this file are not shown. View the raw message.

fs/gfs2/quota.c +1 -0

index 642584265a6f4..95b20e6a3fbc6 100644

Lines of this file are not shown. View the raw message.

fs/hfsplus/bnode.c +1 -1

index c0089849be50e..fb437598e2625 100644

Lines of this file are not shown. View the raw message.

fs/hfsplus/inode.c +11 -1

index 2d68c52f894f9..3f64f68d625c1 100644

Lines of this file are not shown. View the raw message.

fs/hfsplus/super.c +6 -0

index 0831cd7aa5deb..b4c7748c4cf98 100644

Lines of this file are not shown. View the raw message.

fs/iomap/direct-io.c +7 -3

index 52dd8c9c3f6f0..5ccf215f932db 100644

Lines of this file are not shown. View the raw message.

fs/jfs/jfs_logmgr.c +1 -0

index 270808b6219be..a9cfa6307252d 100644

Lines of this file are not shown. View the raw message.

fs/jfs/namei.c +4 -2

index d68a4e6ac3454..e9bd7d3e61e9a 100644

Lines of this file are not shown. View the raw message.

fs/minix/inode.c +29 ~~-21~~

50 lines not on this page · raw message

fs/namespace.c +1 -1

index c3702f3303a89..3869d2b32ac21 100644

Lines of this file are not shown. View the raw message.

fs/nfs/dir.c +2 -2

index 1cf1b2ddbf549..5b90f8727e683 100644

Lines of this file are not shown. View the raw message.

fs/nfs/localio.c +11 ~~-20~~

index 82a053304ad59..84fe3ef21b6da 100644

Lines of this file are not shown. View the raw message.

fs/nfs/pnfs.c +2 -1

index 16981d0389c4c..116499e0f5cee 100644

Lines of this file are not shown. View the raw message.

fs/nfsd/nfs2acl.c +1 -1

index 5fb202acb0fd0..0ac538c761800 100644

Lines of this file are not shown. View the raw message.

fs/nfsd/nfs4idmap.c +46 -6

52 lines not on this page · raw message

fs/nfsd/nfs4proc.c +0 -2

index 05efa10ed84b7..2c7a8943cad9c 100644

Lines of this file are not shown. View the raw message.

fs/nfsd/nfs4xdr.c +16 -0

index fd81db17691a1..b7bdb9b44440b 100644

Lines of this file are not shown. View the raw message.

fs/nfsd/nfsproc.c +1 -1

index 6dda081eb24c0..664171bdefb65 100644

Lines of this file are not shown. View the raw message.

fs/ntfs3/attrib.c +15 -4

index dd459316529e8..4390c0e4bfb78 100644

Lines of this file are not shown. View the raw message.

fs/ntfs3/attrlist.c +9 -0

index a4d74bed74fab..098bd7e8c3d64 100644

Lines of this file are not shown. View the raw message.

fs/ntfs3/file.c +7 -3

index f1122ac5be622..3f144a049d710 100644

Lines of this file are not shown. View the raw message.

fs/ntfs3/fslog.c +3 -0

index d0d530f4e2b95..5afe00972924c 100644

Lines of this file are not shown. View the raw message.

fs/ntfs3/fsntfs.c +6 -0

index 57933576212bb..37c5d9a1f77b7 100644

Lines of this file are not shown. View the raw message.

fs/ntfs3/index.c +6 -1

index 6d1bf890929d9..050b3709e0204 100644

Lines of this file are not shown. View the raw message.

fs/ocfs2/xattr.c +4 -0

index 73a6f6fd8a8ef..b1a18a944c850 100644

Lines of this file are not shown. View the raw message.

fs/overlayfs/readdir.c +1 -1

index 0ca8af060b0c1..e185f4f668b54 100644

Lines of this file are not shown. View the raw message.

fs/proc/array.c +1 -1

index 5e4f7b411fbdb..363d9331216b9 100644

Lines of this file are not shown. View the raw message.

fs/proc/task_mmu.c +2 -1

index c5c1ad791c13e..fb01a071b83d7 100644

Lines of this file are not shown. View the raw message.

fs/pstore/ram_core.c +18 -0

index f1848cdd6d348..7b6d6378a3b87 100644

Lines of this file are not shown. View the raw message.

fs/quota/quota.c +1 -0

index 290157bc7bec2..04c6712d4031c 100644

Lines of this file are not shown. View the raw message.

fs/smb/client/cached_dir.c +2 -2

index e92a61e934e44..d83161285a175 100644

Lines of this file are not shown. View the raw message.

fs/smb/client/connect.c +2 -0

index 3b0f63e0a2534..3c83bda8298ee 100644

Lines of this file are not shown. View the raw message.

fs/smb/client/smb2file.c +2 -0

index 414242a33d61a..b7ab18d4bedca 100644

Lines of this file are not shown. View the raw message.

fs/smb/client/smb2misc.c +3 -3

index cddf273c14aed..5a820176b6f04 100644

Lines of this file are not shown. View the raw message.

fs/smb/client/smb2ops.c +13 ~~-16~~

index 4e7e6ad79966e..ab7e4c9f556f6 100644

Lines of this file are not shown. View the raw message.

fs/smb/client/smb2pdu.c +3 -0

index b0ff9f7e8cea8..23e61ecf1b51c 100644

Lines of this file are not shown. View the raw message.

fs/smb/client/smbdirect.c +17 -2

index b1548269c308a..07f71a9481a36 100644

Lines of this file are not shown. View the raw message.

fs/smb/client/trace.h +1 -0

index 9c3cc7c3300c2..fb9c631e0ec1e 100644

Lines of this file are not shown. View the raw message.

fs/tests/exec_kunit.c +0 -6

index 7c77d039680bb..f412d1a0f6bba 100644

Lines of this file are not shown. View the raw message.

fs/xfs/libxfs/xfs_attr.c +24 ~~-51~~

75 lines not on this page · raw message

fs/xfs/libxfs/xfs_attr_leaf.c +41 -8

49 lines not on this page · raw message

fs/xfs/scrub/agheader_repair.c +6 -2

index 69b003259784f..a93686df6f67b 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/alloc_repair.c +15 -0

index 30295898cc8a6..b43b45fec4f59 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/attr.c +31 ~~-28~~

59 lines not on this page · raw message

fs/xfs/scrub/attr_repair.c +4 -2

index 09d63aa10314b..50ab476dddb98 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/btree.c +2 -0

index b8d5a02334b88..d2b43793f0ef5 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/common.c +7 -0

index 22f5f1a9d3f09..d1b0c8b3a3216 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/dabtree.c +2 -0

index 056de4819f866..a6a5d3a75d994 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/dir_repair.c +6 -2

index 64679fe084465..a9e2aa5c3968d 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/dirtree.c +6 -2

index bde58fb561ea1..73d40a2600a2a 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/ialloc_repair.c +17 -3

index c8d2196a04e15..6cb2c9d115092 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/nlinks.c +2 -1

index 02f5522552dbf..7e917a5e9ca29 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/repair.c +3 -0

index 155bbaaa496e4..c19abc687072f 100644

Lines of this file are not shown. View the raw message.

fs/xfs/scrub/scrub.c +1 -1

index 5c266d2842dbe..9bcea8cbb7a61 100644

Lines of this file are not shown. View the raw message.

include/acpi/ghes.h +1 -0

index be1dd4c1a9174..16646fdd1f841 100644

Lines of this file are not shown. View the raw message.

include/asm-generic/audit_change_attr.h +3 -0

index 331670807cf01..6c311d4d37f4e 100644

Lines of this file are not shown. View the raw message.

include/asm-generic/audit_read.h +6 -0

index 7bb7b5a83ae2e..fb9991f53fb6f 100644

Lines of this file are not shown. View the raw message.

include/drm/drm_of.h +3 -0

index 02d1cdd7f798c..f751f536a6895 100644

Lines of this file are not shown. View the raw message.

include/linux/audit.h +0 -6

index e3f06eba9c6e6..73fb8a4bcf2ae 100644

Lines of this file are not shown. View the raw message.

include/linux/audit_arch.h +7 -0

index 0e34d673ef171..2b8153791e6a5 100644

Lines of this file are not shown. View the raw message.

include/linux/bio.h +2 -0

index 1289b8e487801..80ca2fb879504 100644

Lines of this file are not shown. View the raw message.

include/linux/capability.h +6 -0

index 0c356a5179917..767c535dbd38e 100644

Lines of this file are not shown. View the raw message.

include/linux/clk.h +24 ~~-24~~

48 lines not on this page · raw message

include/linux/compiler_types.h +16 -7

index 8e41eff78f42d..bf775396d384e 100644

Lines of this file are not shown. View the raw message.

include/linux/cper.h +2 -1

index 3670b866ac119..951291fa50d4f 100644

Lines of this file are not shown. View the raw message.

include/linux/ftrace.h +123 ~~-29~~

152 lines not on this page · raw message

include/linux/ftrace_regs.h new file +38 -0

new file mode 100644
index 0000000000000..bbc1873ca6b8e

Lines of this file are not shown. View the raw message.

include/linux/hw_random.h +2 -0

index b424555753b11..b77bc55a4cf35 100644

Lines of this file are not shown. View the raw message.

include/linux/inetdevice.h +1 -1

index cb5280e6cc219..9c0f263e2cd28 100644

Lines of this file are not shown. View the raw message.

include/linux/interrupt.h +1 -1

index b378fbf885ce3..2125d4d9b44f2 100644

Lines of this file are not shown. View the raw message.

include/linux/mfd/wm8350/core.h +1 -1

index a3241e4d75486..4816d4f472101 100644

Lines of this file are not shown. View the raw message.

include/linux/mlx5/driver.h +2 -2

index 9a8eb644f6707..2e3324578f2ea 100644

Lines of this file are not shown. View the raw message.

include/linux/module.h +9 -0

index 7886217c99881..1cb6f80e1b485 100644

Lines of this file are not shown. View the raw message.

include/linux/mtd/spinand.h +1 -1

index 702e5fb13dae7..4bf33cefbae5f 100644

Lines of this file are not shown. View the raw message.

include/linux/pci_ids.h +1 -0

index c395b3c5c05cf..ba1b9617f724a 100644

Lines of this file are not shown. View the raw message.

include/linux/psp.h +1 -0

index 92e60aeef21e1..b337dcce1e991 100644

Lines of this file are not shown. View the raw message.

include/linux/skbuff.h +32 -0

index 2e26a054d260c..4344724a97821 100644

Lines of this file are not shown. View the raw message.

include/linux/skmsg.h +68 -2

70 lines not on this page · raw message

include/linux/sunrpc/xdrgen/_builtins.h +8 ~~-12~~

index 66ca3ece951ab..a5ab75d2db044 100644

Lines of this file are not shown. View the raw message.

include/linux/trace_events.h +5 -0

index fcf5a64d5cfe2..54ba231ded519 100644

Lines of this file are not shown. View the raw message.

include/linux/u64_stats_sync.h +10 -0

index 457879938fc19..3366090a86bd2 100644

Lines of this file are not shown. View the raw message.

include/media/dvb_vb2.h +4 -2

index 8cb88452cd6c2..0fbbfc65157e6 100644

Lines of this file are not shown. View the raw message.

include/net/bluetooth/l2cap.h +5 -3

index 9189354c568f4..b233779824c20 100644

Lines of this file are not shown. View the raw message.

include/net/ioam6.h +2 -0

index 2cbbee6e806aa..a75912fe247e6 100644

Lines of this file are not shown. View the raw message.

include/net/ipv6.h +9 -6

index 6d52b5584d2fb..e843eb7efbccd 100644

Lines of this file are not shown. View the raw message.

include/net/netfilter/nf_conntrack_count.h +1 -0

index 52a06de41aa0f..cf0166520cf33 100644

Lines of this file are not shown. View the raw message.

include/net/netfilter/nf_queue.h +4 -0

index 4aeffddb75861..45eb26b2e95b3 100644

Lines of this file are not shown. View the raw message.

include/net/netns/ipv4.h +7 -2

index 276f622f35168..a15e9366175ec 100644

Lines of this file are not shown. View the raw message.

include/rdma/rw.h +2 -0

index d606cac482338..9a8f4b76ce588 100644

Lines of this file are not shown. View the raw message.

include/uapi/linux/hyperv.h +1 -1

index aaa502a7bff46..1749b35ab2c21 100644

Lines of this file are not shown. View the raw message.

include/uapi/linux/netfilter_bridge.h +4 -0

index 1610fdbab98df..ad520d3e9df8f 100644

Lines of this file are not shown. View the raw message.

include/uapi/linux/nfs.h +1 -1

index 71c7196d32817..e629c49535345 100644

Lines of this file are not shown. View the raw message.

include/uapi/linux/vbox_vmmdev_types.h +2 -2

index 6073858d52a2e..11f3627c3729b 100644

Lines of this file are not shown. View the raw message.

include/ufs/ufshcd.h +0 -4

index bdc5564b16fba..e68ce42eaff4d 100644

Lines of this file are not shown. View the raw message.

include/xen/xen.h +2 -0

index a1e5b3f18d69f..86fe96fe51834 100644

Lines of this file are not shown. View the raw message.

io_uring/cancel.h +2 -4

index b33995e00ba90..da13a1d820622 100644

Lines of this file are not shown. View the raw message.

io_uring/filetable.c +4 -0

index 6183d61c7222d..72423e27e5e1d 100644

Lines of this file are not shown. View the raw message.

io_uring/io_uring.c +5 -1

index 99b0b1ba0fe22..5c60442e67028 100644

Lines of this file are not shown. View the raw message.

io_uring/msg_ring.c +10 -2

index 97708e5132bc4..3cf59d8c58073 100644

Lines of this file are not shown. View the raw message.

io_uring/net.c +5 -1

index b7c93765fcff8..56a0acc0894c8 100644

Lines of this file are not shown. View the raw message.

io_uring/register.c +2 -1

index a325b493ae121..f700ddf1f1d1f 100644

Lines of this file are not shown. View the raw message.

io_uring/sync.c +2 -0

index 255f68c37e55c..27bd0a26500bc 100644

Lines of this file are not shown. View the raw message.

ipc/ipc_sysctl.c +1 -1

index 54318e0b45578..61ce52ce30530 100644

Lines of this file are not shown. View the raw message.

kernel/bpf/crypto.c +7 -1

index 83c4d9943084b..1d024fe7248ac 100644

Lines of this file are not shown. View the raw message.

kernel/bpf/verifier.c +49 ~~-12~~

61 lines not on this page · raw message

kernel/configs/debug.config +0 -1

index 509ee703de152..c1b15426fef45 100644

Lines of this file are not shown. View the raw message.

kernel/kallsyms.c +2 -2

index 9e4bf061bb834..9d3f0c1cca8e2 100644

Lines of this file are not shown. View the raw message.

kernel/kexec_file.c +74 ~~-57~~

131 lines not on this page · raw message

kernel/module/kallsyms.c +2 -7

index bf65e0c3c86fc..30d0798f114f1 100644

Lines of this file are not shown. View the raw message.

kernel/rcu/tree.h +1 -1

index 8ba04b179416a..08c020e01425d 100644

Lines of this file are not shown. View the raw message.

kernel/rcu/tree_plugin.h +82 ~~-17~~

99 lines not on this page · raw message

kernel/sched/deadline.c +3 -0

index 1689d190dea8f..8acdd97538546 100644

Lines of this file are not shown. View the raw message.

kernel/sched/debug.c +4 -3

index 72958b31549fb..7d14e9fa53ac3 100644

Lines of this file are not shown. View the raw message.

kernel/sched/rt.c +5 -0

index c437a15026238..ffcce501ed40c 100644

Lines of this file are not shown. View the raw message.

kernel/time/hrtimer.c +1 -1

index 184d5c3d89bac..640d2ea4bd1fa 100644

Lines of this file are not shown. View the raw message.

kernel/trace/Kconfig +2 -2

index 721c3b221048a..ab277eff80dc2 100644

Lines of this file are not shown. View the raw message.

kernel/trace/fgraph.c +21 ~~-14~~

index 910da0e4531ae..c2d9937158117 100644

Lines of this file are not shown. View the raw message.

kernel/trace/ftrace.c +5 -2

index b2442aabccfd0..c8a6c0bb907ea 100644

Lines of this file are not shown. View the raw message.

kernel/trace/ring_buffer.c +5 -1

index 2c42e26ced6b6..9e72543e0099b 100644

Lines of this file are not shown. View the raw message.

kernel/trace/trace.c +1 -1

index 2f68e6341703c..fb76a7262abf8 100644

Lines of this file are not shown. View the raw message.

kernel/trace/trace_events.c +3 -5

index a3d7067eae654..38218cfe20e90 100644

Lines of this file are not shown. View the raw message.

kernel/trace/trace_events_hist.c +3 -3

index 761d56ed9b8e5..83de1a196a4af 100644

Lines of this file are not shown. View the raw message.

kernel/trace/trace_hwlat.c +7 -8

index 3bd6071441ade..bc437b6ce8969 100644

Lines of this file are not shown. View the raw message.

kernel/ucount.c +1 -1

index 78f4c4255358f..8340f767c1aea 100644

Lines of this file are not shown. View the raw message.

kernel/watchdog.c +1 -1

index 8fbb4385e8149..70cb35d5420d8 100644

Lines of this file are not shown. View the raw message.

kernel/workqueue.c +73 ~~-19~~

92 lines not on this page · raw message

lib/Kconfig.debug +0 ~~-27~~

index b1d7c427bbe3d..ffa3da3583537 100644

Lines of this file are not shown. View the raw message.

lib/objpool.c +1 -1

index b998b720c7329..d98fadf1de169 100644

Lines of this file are not shown. View the raw message.

mm/highmem.c +2 -1

index ef3189b36cadb..baade043c2148 100644

Lines of this file are not shown. View the raw message.

mm/numa_memblks.c +5 -4

index c447add277ccd..108736d6b3aea 100644

Lines of this file are not shown. View the raw message.

mm/page_alloc.c +14 -0

index f30a4ab8f254c..4282c9d0a5ddd 100644

Lines of this file are not shown. View the raw message.

mm/slub.c +7 -7

index 30c544a0709e8..a6ed12d3e0449 100644

Lines of this file are not shown. View the raw message.

mm/vmalloc.c +8 -0

index 26e5ab2edaea3..1d2262fb54185 100644

Lines of this file are not shown. View the raw message.

net/9p/trans_xen.c +44 ~~-41~~

85 lines not on this page · raw message

net/atm/signaling.c +54 -2

56 lines not on this page · raw message

net/bluetooth/hci_conn.c +3 -2

index dad9020474149..fa74fac5af778 100644

Lines of this file are not shown. View the raw message.

net/bluetooth/hci_sync.c +0 -2

index f79b38603205c..00de90fee44a7 100644

Lines of this file are not shown. View the raw message.

net/bluetooth/l2cap_core.c +70 ~~-25~~

95 lines not on this page · raw message

net/bluetooth/l2cap_sock.c +11 -4

index b35f1551b9be7..ef1b8a44420ed 100644

Lines of this file are not shown. View the raw message.

net/bridge/br_multicast.c +18 ~~-27~~

45 lines not on this page · raw message

net/ceph/crypto.c +5 -3

index 051d22c0e4ad4..3397d105f74f9 100644

Lines of this file are not shown. View the raw message.

net/ceph/crypto.h +1 -1

index 13bd526349fa1..0d32f1649f3d0 100644

Lines of this file are not shown. View the raw message.

net/ceph/messenger_v2.c +1 -1

index f163283abc4e9..83c29714226fd 100644

Lines of this file are not shown. View the raw message.

net/core/dev.c +19 -6

index 1d276a26a360d..e7127eca1afc5 100644

Lines of this file are not shown. View the raw message.

net/core/filter.c +1 -1

index 06e179865a21b..182a7388e84f5 100644

Lines of this file are not shown. View the raw message.

net/core/gro.c +1 -1

index 40aaac4e04f34..ac498c9f82cf5 100644

Lines of this file are not shown. View the raw message.

net/core/skmsg.c +27 -3

index adb3166ede972..6ece4eaecd489 100644

Lines of this file are not shown. View the raw message.

net/ipv4/fib_lookup.h +4 -2

index f9b9e26c32c19..0b72796dd1ad3 100644

Lines of this file are not shown. View the raw message.

net/ipv4/fib_trie.c +2 -2

index 658f26d9a9ec5..ee47b67a08703 100644

Lines of this file are not shown. View the raw message.

net/ipv4/icmp.c +31 -8

index 508b23204edc5..8ab51b51cc9b2 100644

Lines of this file are not shown. View the raw message.

net/ipv4/igmp.c +2 -2

index f4a87b90351e9..52c661c6749f3 100644

Lines of this file are not shown. View the raw message.

net/ipv4/ip_options.c +2 -3

index 81e86e5defee6..3d154bc7e1f2e 100644

Lines of this file are not shown. View the raw message.

net/ipv4/ping.c +19 ~~-12~~

index f62b17f59bb4a..0089c1605acfe 100644

Lines of this file are not shown. View the raw message.

net/ipv4/tcp.c +3 -0

index ad5f30cefdf96..4090107b0c4d5 100644

Lines of this file are not shown. View the raw message.

net/ipv4/tcp_bpf.c +23 -2

index 8372ca512a755..f5817438f1734 100644

Lines of this file are not shown. View the raw message.

net/ipv4/udp_bpf.c +19 -4

index 0735d820e413f..91233e37cd97a 100644

Lines of this file are not shown. View the raw message.

net/ipv6/af_inet6.c +2 -2

index f60ec8b0f8ea4..0786155715249 100644

Lines of this file are not shown. View the raw message.

net/ipv6/exthdrs.c +11 -4

index 20f77fdfb73da..1a627c24e4c30 100644

Lines of this file are not shown. View the raw message.

net/ipv6/icmp.c +8 -1

index 13a796bfc2f93..e43b49f1ddbb2 100644

Lines of this file are not shown. View the raw message.

net/ipv6/ioam6.c +14 -0

index 08c9295130657..b6ed67d7027c1 100644

Lines of this file are not shown. View the raw message.

net/ipv6/ioam6_iptunnel.c +1 -9

index 9e4774771023b..7cbff7a0501bb 100644

Lines of this file are not shown. View the raw message.

net/ipv6/ip6_fib.c +1 -1

index d83430f4a0eff..01c953a39211a 100644

Lines of this file are not shown. View the raw message.

net/ipv6/tcp_ipv6.c +2 -1

index 06edfe0b2db90..c90b20c218bff 100644

Lines of this file are not shown. View the raw message.

net/ipv6/xfrm6_policy.c +5 -2

index 1f19b6f14484c..125ea9a5b8a08 100644

Lines of this file are not shown. View the raw message.

net/kcm/kcmsock.c +19 -2

index 1d37b26ea2ef7..4e34311b27b18 100644

Lines of this file are not shown. View the raw message.

net/mptcp/protocol.c +4 -4

index f2bf78c019df4..e682d52a06b7e 100644

Lines of this file are not shown. View the raw message.

net/mptcp/protocol.h +5 -0

index bdec5ad9defb9..b266002660d70 100644

Lines of this file are not shown. View the raw message.

net/netfilter/ipvs/ip_vs_xmit.c +36 ~~-10~~

46 lines not on this page · raw message

net/netfilter/nf_conncount.c +40 ~~-14~~

54 lines not on this page · raw message

net/netfilter/nf_conntrack_h323_asn1.c +1 -1

index 540d97715bd23..62aa22a078769 100644

Lines of this file are not shown. View the raw message.

net/netfilter/nf_conntrack_h323_main.c +5 -5

index 5a9bce24f3c3d..ed983421e2eb2 100644

Lines of this file are not shown. View the raw message.

net/netfilter/nf_conntrack_proto_generic.c +1 -0

index e831637bc8ca8..cb260eb3d012c 100644

Lines of this file are not shown. View the raw message.

net/netfilter/nf_tables_api.c +13 -0

index 3bf88c137868a..8dccd3598166b 100644

Lines of this file are not shown. View the raw message.

net/netfilter/nfnetlink_queue.c +189 ~~-78~~

267 lines not on this page · raw message

net/netfilter/nft_compat.c +10 -3

index 72711d62fddfa..08f620311b03f 100644

Lines of this file are not shown. View the raw message.

net/netfilter/nft_connlimit.c +1 -6

index 83a7d5769396c..5dd50b3ab5a45 100644

Lines of this file are not shown. View the raw message.

net/netfilter/nft_counter.c +2 -2

index cc73253294963..0d70325280cc5 100644

Lines of this file are not shown. View the raw message.

net/netfilter/nft_set_hash.c +7 -2

index 900eddb93dcc8..e87398cefef00 100644

Lines of this file are not shown. View the raw message.

net/netfilter/nft_set_rbtree.c +38 -5

43 lines not on this page · raw message

net/netfilter/xt_tcpmss.c +1 -1

index 37704ab017992..0d32d4841cb32 100644

Lines of this file are not shown. View the raw message.

net/nfc/hci/llc_shdlc.c +8 -0

index e90f70385813a..a106f4352356d 100644

Lines of this file are not shown. View the raw message.

net/nfc/nci/ntf.c +141 ~~-18~~

159 lines not on this page · raw message

net/rds/connection.c +4 -0

index c749c5525b40f..3a1b548dcdcb2 100644

Lines of this file are not shown. View the raw message.

net/rds/send.c +4 -2

index 09a2801106549..4a24ee9c22d7c 100644

Lines of this file are not shown. View the raw message.

net/rds/tcp_listen.c +0 -5

index d89bd8d0c3545..fced9e286f79f 100644

Lines of this file are not shown. View the raw message.

net/sched/act_skbedit.c +5 -1

index 1f1d9ce3e968a..2680196b09d0d 100644

Lines of this file are not shown. View the raw message.

net/sunrpc/auth_gss/auth_gss.c +3 -0

index 369310909fc98..785d53a612426 100644

Lines of this file are not shown. View the raw message.

net/sunrpc/auth_gss/gss_rpc_xdr.c +64 ~~-18~~

82 lines not on this page · raw message

net/sunrpc/xprtrdma/svc_rdma_transport.c +6 -2

index 3d7f1413df023..12857381e8610 100644

Lines of this file are not shown. View the raw message.

net/tipc/crypto.c +1 -1

index 2721baf9fd2b3..d7736d9002715 100644

Lines of this file are not shown. View the raw message.

net/tipc/name_table.c +4 -2

index d1180370fdf41..e6555254ddb85 100644

Lines of this file are not shown. View the raw message.

net/tls/tls_sw.c +1 -1

index 1ff0d01bdadf0..bf01155b1011a 100644

Lines of this file are not shown. View the raw message.

net/vmw_vsock/vmci_transport.c +1 -1

index 7eccd6708d664..aca3132689cf1 100644

Lines of this file are not shown. View the raw message.

net/wireless/core.c +5 -7

index 6bb8a7037d24d..73c051f129d33 100644

Lines of this file are not shown. View the raw message.

net/wireless/scan.c +1 -1

index f00ccc6d803be..f9aff1c58e800 100644

Lines of this file are not shown. View the raw message.

net/wireless/wext-compat.c +1 -1

index 2371069f3c432..3af11dae0942a 100644

Lines of this file are not shown. View the raw message.

net/xfrm/espintcp.c +1 -1

index fc7a603b04f13..a591df9253526 100644

Lines of this file are not shown. View the raw message.

net/xfrm/xfrm_device.c +11 -1

index 32ad8f3fc81e8..7744ed8e4c83f 100644

Lines of this file are not shown. View the raw message.

net/xfrm/xfrm_policy.c +9 -2

index 2c42d83fbaa2d..aba06ff8694de 100644

Lines of this file are not shown. View the raw message.

rust/Makefile +3 -0

index c5571bab1bf5b..9c11b11a11d4f 100644

Lines of this file are not shown. View the raw message.

scripts/mod/modpost.c +4 -0

index 971eda0c6ba73..07e8a4eb71d04 100644

Lines of this file are not shown. View the raw message.

security/apparmor/apparmorfs.c +9 -0

index 01b923d97a446..584b40718ecb7 100644

Lines of this file are not shown. View the raw message.

security/apparmor/include/match.h +7 -5

index ae31a8a631fc6..dfc93631b43d8 100644

Lines of this file are not shown. View the raw message.

security/apparmor/label.c +14 ~~-19~~

index c71e4615dd460..af25ca6b6b83f 100644

Lines of this file are not shown. View the raw message.

security/apparmor/lsm.c +2 -1

index 9a78fd36542d6..8855fb4b88342 100644

Lines of this file are not shown. View the raw message.

security/apparmor/match.c +11 ~~-11~~

index 12e036f8ce0f7..fae26953619a7 100644

Lines of this file are not shown. View the raw message.

security/apparmor/net.c +4 -2

index 77413a5191179..f6f749191f601 100644

Lines of this file are not shown. View the raw message.

security/apparmor/policy_unpack.c +4 -2

index 3483c595f999f..8f7d6ff5aef60 100644

Lines of this file are not shown. View the raw message.

security/apparmor/resource.c +5 -0

index dcc94c3153d51..a7eee815f1215 100644

Lines of this file are not shown. View the raw message.

security/integrity/evm/evm_crypto.c +10 -4

index 7c06ffd633d24..c588af7cc5f87 100644

Lines of this file are not shown. View the raw message.

security/smack/smackfs.c +50 ~~-29~~

79 lines not on this page · raw message

sound/core/oss/mixer_oss.c +16 -0

index 05fc8911479c1..a6cc74bb25fd4 100644

Lines of this file are not shown. View the raw message.

sound/core/pcm.c +2 -2

index 290690fc2abcb..ff1e9f8c1ecae 100644

Lines of this file are not shown. View the raw message.

sound/core/pcm_compat.c +5 -4

index a42ec7f5a1daf..c1c64da2eabd0 100644

Lines of this file are not shown. View the raw message.

sound/core/pcm_native.c +25 ~~-23~~

48 lines not on this page · raw message

sound/core/vmaster.c +6 -6

index c657659b236c4..76cc64245f5df 100644

Lines of this file are not shown. View the raw message.

sound/pci/hda/patch_conexant.c +1 -0

index 84ab357b840d6..482e801a496a1 100644

Lines of this file are not shown. View the raw message.

sound/pci/hda/patch_realtek.c +205 -0

205 lines not on this page · raw message

sound/soc/amd/yc/acp6x-mach.c +7 -1

index 6d073ecad6f02..f33946fb895da 100644

Lines of this file are not shown. View the raw message.

sound/soc/codecs/aw88261.c +2 -1

index fb99871578c5a..38f362b022aa3 100644

Lines of this file are not shown. View the raw message.

sound/soc/codecs/es8328.c +8 -2

index 76159c45e6b52..c0d7ce64b2d96 100644

Lines of this file are not shown. View the raw message.

sound/soc/codecs/max98390.c +3 -0

index 1bae253618fd0..3a2befb3fab39 100644

Lines of this file are not shown. View the raw message.

sound/soc/codecs/nau8821.c +47 ~~-38~~

85 lines not on this page · raw message

sound/soc/codecs/nau8821.h +2 -1

index f0935ffafcbec..f9d7cd8cbd211 100644

Lines of this file are not shown. View the raw message.

sound/soc/codecs/wm8962.c +11 -1

index 08d164ce3e49c..95143472c9e4f 100644

Lines of this file are not shown. View the raw message.

sound/soc/fsl/fsl_xcvr.c +0 -3

index d6f00920391d1..656a4d619cdf1 100644

Lines of this file are not shown. View the raw message.

sound/soc/fsl/imx-rpmsg.c +1 -1

index ce98d2288193b..b4d6ad563445f 100644

Lines of this file are not shown. View the raw message.

sound/soc/intel/common/soc-acpi-intel-arl-match.c +11 ~~-12~~

index 1ad704ca2c5f2..36d73623fb161 100644

Lines of this file are not shown. View the raw message.

sound/soc/rockchip/rockchip_i2s_tdm.c +10 -0

index 7feefeb6b876d..46c338ddefe9f 100644

Lines of this file are not shown. View the raw message.

sound/soc/sof/intel/hda-dai.c +12 -2

index 2e58a264da556..169bfd23f1b93 100644

Lines of this file are not shown. View the raw message.

sound/soc/sof/ipc4-control.c +32 -9

41 lines not on this page · raw message

sound/soc/sof/ipc4-topology.c +27 -8

index 4849a3ce02dca..9208cbe95e3c9 100644

Lines of this file are not shown. View the raw message.

sound/soc/sof/ipc4.c +42 -2

44 lines not on this page · raw message

sound/soc/sunxi/sun50i-dmic.c +3 -0

index 3e751b5694fe3..e8e03a5e35bc7 100644

Lines of this file are not shown. View the raw message.

sound/usb/endpoint.c +23 ~~-17~~

index aa201e4744bf6..cb94c2cad2213 100644

Lines of this file are not shown. View the raw message.

sound/usb/quirks.c +2 -0

index 8fa840df46210..947467112409a 100644

Lines of this file are not shown. View the raw message.

tools/bpf/bpftool/net.c +4 -1

index 39f208928cdb5..587403a19af3a 100644

Lines of this file are not shown. View the raw message.

tools/include/linux/bitfield.h +1 -0

index 6093fa6db2600..ddf81f24956ba 100644

Lines of this file are not shown. View the raw message.

tools/lib/bpf/btf_dump.c +9 -0

index 12306b5de3efb..a833d91886f87 100644

Lines of this file are not shown. View the raw message.

tools/lib/bpf/netlink.c +3 -1

index 68a2def171751..6f16c4f7b3a43 100644

Lines of this file are not shown. View the raw message.

tools/lib/perf/Makefile +4 ~~-10~~

index 3a9b2140aa048..703a8ff0b3430 100644

Lines of this file are not shown. View the raw message.

tools/lib/subcmd/help.c +6 -4

index ddaeb4eb3e249..db94aa685b73b 100644

Lines of this file are not shown. View the raw message.

tools/net/sunrpc/xdrgen/generators/__init__.py +2 -1

index fd24574612742..49191cd10ab70 100644

Lines of this file are not shown. View the raw message.

tools/net/sunrpc/xdrgen/templates/C/program/decoder/argument.j2 +4 -0

index 0b1709cca0d4a..19b219dd276d3 100644

Lines of this file are not shown. View the raw message.

tools/net/sunrpc/xdrgen/templates/C/program/encoder/result.j2 +6 -0

index 6fc61a5d47b7f..746592cfda562 100644

Lines of this file are not shown. View the raw message.

tools/objtool/Makefile +2 -0

index bf7f7f84ac625..02d1fccd495f4 100644

Lines of this file are not shown. View the raw message.

tools/perf/pmu-events/arch/x86/amdzen5/load-store.json +3 -3

index af2fdf1f55d64..917f9d68f85a6 100644

Lines of this file are not shown. View the raw message.

tools/perf/tests/shell/stat.sh +3 -3

index 62f13dfeae8e4..a76ccf2deb563 100755

Lines of this file are not shown. View the raw message.

tools/perf/util/disasm.c +1 -1

index a228a7ba30caa..2dc93199ac258 100644

Lines of this file are not shown. View the raw message.

tools/perf/util/evsel_fprintf.c +6 -2

index c2c0500d5da99..2108e02d4b6cd 100644

Lines of this file are not shown. View the raw message.

tools/perf/util/maps.c +1 -0

index 09c9cc326c08d..67133b60b03cd 100644

Lines of this file are not shown. View the raw message.

tools/perf/util/unwind-libdw.c +5 -2

index bde216e630d29..216f0d3762fda 100644

Lines of this file are not shown. View the raw message.

tools/power/cpupower/lib/cpuidle.c +1 -0

index f2c1139adf716..bd857ee7541a7 100644

Lines of this file are not shown. View the raw message.

tools/power/x86/intel-speed-select/isst-config.c +2 -0

index 5127be34869eb..07729d376f018 100644

Lines of this file are not shown. View the raw message.

tools/spi/.gitignore +1 -0

index 14ddba3d21957..038261b34ed83 100644

Lines of this file are not shown. View the raw message.

tools/testing/selftests/bpf/prog_tests/wq.c +3 -2

index 99e438fe12acd..15ac8e6d17450 100644

Lines of this file are not shown. View the raw message.

tools/testing/selftests/bpf/veristat.c +1 -1

index 7b6b9c4cadb57..e9d7acff6bbbc 100644

Lines of this file are not shown. View the raw message.

tools/testing/selftests/drivers/net/mlxsw/tc_restrictions.sh +2 -2

index 0441a18f098b1..aac8ef490feb8 100755

Lines of this file are not shown. View the raw message.

tools/testing/selftests/memfd/memfd_test.c +105 -8

113 lines not on this page · raw message

tools/testing/selftests/mm/charge_reserved_hugetlb.sh +2 -2

index e1fe16bcbbe88..fa6713892d82d 100755

Lines of this file are not shown. View the raw message.

tools/testing/selftests/mm/pagemap_ioctl.c +62 ~~-54~~

116 lines not on this page · raw message

tools/testing/selftests/mm/vm_util.c +1 -1

index a4a2805d3d3e7..4fa66a50e81a4 100644

Lines of this file are not shown. View the raw message.

tools/testing/selftests/net/forwarding/vxlan_bridge_1d.sh +16 ~~-10~~

index 3f9d50f1ef9ec..1952023c43ba4 100755

Lines of this file are not shown. View the raw message.

tools/testing/selftests/net/forwarding/vxlan_bridge_1d_ipv6.sh +1 -1

index a603f7b0a08f0..e642feeada0e7 100755

Lines of this file are not shown. View the raw message.

The rest of this diff is not shown. View the raw message.

Part of the diff is not shown here. View the raw message.

Vitaly Chikunov

2026-04-02 08:53 UTC #2 lore raw

Sasha,

1. I cannot find this commit posted on lore.kernel.org to report to exact patch.

| From: Matt Roper <[email protected]>
| Date: Tue, 10 Sep 2024 16:47:29 -0700
| Subject: [PATCH 6.12/sisyphus] drm/xe: Switch MMIO interface to take xe_mmio
|  instead of xe_gt
| 
| [ Upstream commit a84590c5ceb354d2e9f7f6812cfb3a9709e14afa ]
| 
| Since much of the MMIO register access done by the driver is to non-GT
| registers, use of 'xe_gt' in these interfaces has been a long-standing
| design flaw that's been hard to disentangle.
| 
| To avoid a flag day across the whole driver, munge the function names
| and add temporary compatibility macros with the original function names
| that can accept either the new xe_mmio or the old xe_gt structure as a
| parameter.  This will allow us to slowly convert parts of the driver
| over to the new interface independently.
| 
| Signed-off-by: Matt Roper <[email protected]>
| Reviewed-by: Rodrigo Vivi <[email protected]>
| Link: https://patchwork.freedesktop.org/patch/msgid/[email protected]
| Stable-dep-of: 4a9b4e1fa52a ("drm/xe/mmio: Avoid double-adjust in 64-bit reads")
| Signed-off-by: Sasha Levin <[email protected]>
| ---
|  drivers/gpu/drm/xe/xe_mmio.h  |  72 +++++++++++++++----
|  drivers/gpu/drm/xe/xe_trace.h |   7 +-
|  drivers/gpu/drm/xe/xe_mmio.c  | 131 ++++++++++++++++------------------
|  3 files changed, 124 insertions(+), 86 deletions(-)

2. After this patch applied to 6.12.75 there is kernel NULL pointer dereference BUG on MSI MAG H670 12th Gen Intel(R) Core(TM) i5-12600K with ASRock Intel Arc B580 Challenger [Alchemist], 12GB:

  BUG: kernel NULL pointer dereference, address: 0000000000000000
  #PF: supervisor read access in kernel mode
  #PF: error_code(0x0000) - not-present page
  PGD 0 P4D 0
  Oops: Oops: 0000 [#1] PREEMPT SMP NOPTI
  CPU: 8 UID: 0 PID: 310 Comm: (udev-worker) Not tainted 6.12.79-6.12-alt1 #1
  Hardware name: Micro-Star International Co., Ltd. MS-7D25/MAG H670 TOMAHAWK WIFI DDR4(MS-7D25), BIOS H.N0 07/31/2025
  RIP: 0010:__xe_mmio_read32+0x23/0xe0 [xe]

The commit is found not by a git bisect (since it's reported by end user and I cannot reproduce it on my hardware) but (by analyzing dmesg) with:

(gdb) list *__xe_mmio_read32+0x23
0x35723 is in __xe_mmio_read32 (drivers/gpu/drm/xe/xe_mmio.c:195).

  190     static void mmio_flush_pending_writes(struct xe_mmio *mmio)
  191     {
  192     #define DUMMY_REG_OFFSET        0x130030

193 int i;
194
195 if (mmio->tile->xe->info.platform != XE_LUNARLAKE)
196 return;
197
198 /* 4 dummy writes */
199 for (i = 0; i < 4; i++)

Then finding the suspecting commit:

  $ git log --oneline -G'XE_LUNARLAKE' v6.12.74..v6.12.75
  26a40327c25c drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt

6.18 and above are not affected by the bug. Also, they have another commit modifying the line which is not present in 6.12 branch:

ac596dee8008 drm/xe: Move Wa_15015404425 to use the new XE_DEVICE_WA macro

Thanks,

#regzbot introduced: v6.12.75

Quoted 22 lines · Sasha Levin

drivers/gpu/drm/xe/xe_mmio.c +3 -4

index 3fd462fda6255..449e6c5636712 100644
@@ -172,122 +180,118 @@ int xe_mmio_init(struct xe_device *xe)
-static void mmio_flush_pending_writes(struct xe_gt *gt)
+static void mmio_flush_pending_writes(struct xe_mmio *mmio)
 {
 #define DUMMY_REG_OFFSET	0x130030
-	struct xe_tile *tile = gt_to_tile(gt);
 	int i;
 
-	if (tile->xe->info.platform != XE_LUNARLAKE)
+	if (mmio->tile->xe->info.platform != XE_LUNARLAKE)
 		return;
 
 	/* 4 dummy writes */
 	for (i = 0; i < 4; i++)
-		writel(0, tile->mmio.regs + DUMMY_REG_OFFSET);
+		writel(0, mmio->regs + DUMMY_REG_OFFSET);
 }

Thorsten Leemhuis

2026-04-13 11:33 UTC #3 lore raw

Quoted 27 lines · Vitaly Chikunov

Sasha,
1. I cannot find this commit posted on lore.kernel.org to report to exact patch.
| From: Matt Roper <[email protected]>
| Date: Tue, 10 Sep 2024 16:47:29 -0700
| Subject: [PATCH 6.12/sisyphus] drm/xe: Switch MMIO interface to take xe_mmio
|  instead of xe_gt
| 
| [ Upstream commit a84590c5ceb354d2e9f7f6812cfb3a9709e14afa ]
| 
| Since much of the MMIO register access done by the driver is to non-GT
| registers, use of 'xe_gt' in these interfaces has been a long-standing
| design flaw that's been hard to disentangle.
[...]
2. After this patch applied to 6.12.75 there is kernel NULL pointer dereference BUG on MSI MAG H670 12th Gen Intel(R) Core(TM) i5-12600K with ASRock Intel Arc B580 Challenger [Alchemist], 12GB:
[...]
The commit is found not by a git bisect (since it's reported by end user and I cannot reproduce it on my hardware) but (by analyzing dmesg) with:
[...]
Then finding the suspecting commit:

Quoted 7 lines

  $ git log --oneline -G'XE_LUNARLAKE' v6.12.74..v6.12.75
  26a40327c25c drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt
6.18 and above are not affected by the bug. Also, they have another commit modifying the line which is not present in 6.12 branch:
[...]
Related drm/xe bug report https://gitlab.freedesktop.org/drm/xe/kernel/-/work_items/7661

Nobody reacted to this and it seems the gitlab ticket is stalled, too. So let me ask: can this be resolved by reverting 26a40327c25c in 6.12.y?

Ciao, Thorsten

Vitaly Chikunov

2026-04-13 14:24 UTC #4 lore raw

Thorsten, Sasha,

Quoted 31 lines · Thorsten Leemhuis

Quoted 30 lines · Vitaly Chikunov
Sasha,
1. I cannot find this commit posted on lore.kernel.org to report to exact patch.
| From: Matt Roper <[email protected]>
| Date: Tue, 10 Sep 2024 16:47:29 -0700
| Subject: [PATCH 6.12/sisyphus] drm/xe: Switch MMIO interface to take xe_mmio
|  instead of xe_gt
| 
| [ Upstream commit a84590c5ceb354d2e9f7f6812cfb3a9709e14afa ]
| 
| Since much of the MMIO register access done by the driver is to non-GT
| registers, use of 'xe_gt' in these interfaces has been a long-standing
| design flaw that's been hard to disentangle.
[...]
2. After this patch applied to 6.12.75 there is kernel NULL pointer dereference BUG on MSI MAG H670 12th Gen Intel(R) Core(TM) i5-12600K with ASRock Intel Arc B580 Challenger [Alchemist], 12GB:
[...]
The commit is found not by a git bisect (since it's reported by end user and I cannot reproduce it on my hardware) but (by analyzing dmesg) with:
[...]
Then finding the suspecting commit:
  $ git log --oneline -G'XE_LUNARLAKE' v6.12.74..v6.12.75
  26a40327c25c drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt

Quoted 6 lines

Quoted 4 lines
6.18 and above are not affected by the bug. Also, they have another commit modifying the line which is not present in 6.12 branch:
[...]
Related drm/xe bug report https://gitlab.freedesktop.org/drm/xe/kernel/-/work_items/7661
Nobody reacted to this and it seems the gitlab ticket is stalled, too. So let me ask: can this be resolved by reverting 26a40327c25c in 6.12.y?

As of me, this is not easy to revert, as it depends on many other commits, and git does not have tooling to determine all dependant commits for revert. I hope someone from drm subsystem notices this to work on it, or Sasha can pull missing commits or revert this (obviously, he have tooling for this, but I was unable to find it). [I found obsolete references to deps but is seems not used for years and Python git-deps tool seems broken.]

What I found is, offending commit is picked due to

Stable-dep-of: 4a9b4e1fa52a ("drm/xe/mmio: Avoid double-adjust in 64-bit reads")

Which, perhaps, needs to be reverted.

Offending commit 26a40327c25c is not tracked in lore.
It's part of 9 piece patchset, perhaps they are logically dependent too, so need to be reverted together.

The possible fix is part of 6 piece patchset, which does not cherry-pick easily due to conflicts.

If someone can produce correct fix we can participate in the tests.

Thanks,

Quoted 2 lines

Ciao, Thorsten

Vitaly Chikunov

2026-04-14 00:17 UTC #5 lore raw

Thorsten,

Quoted 40 lines · Vitaly Chikunov

Thorsten, Sasha,
Quoted 37 lines · Thorsten Leemhuis
Quoted 27 lines · Vitaly Chikunov
Sasha,
1. I cannot find this commit posted on lore.kernel.org to report to exact patch.
| From: Matt Roper <[email protected]>
| Date: Tue, 10 Sep 2024 16:47:29 -0700
| Subject: [PATCH 6.12/sisyphus] drm/xe: Switch MMIO interface to take xe_mmio
|  instead of xe_gt
| 
| [ Upstream commit a84590c5ceb354d2e9f7f6812cfb3a9709e14afa ]
| 
| Since much of the MMIO register access done by the driver is to non-GT
| registers, use of 'xe_gt' in these interfaces has been a long-standing
| design flaw that's been hard to disentangle.
[...]
2. After this patch applied to 6.12.75 there is kernel NULL pointer dereference BUG on MSI MAG H670 12th Gen Intel(R) Core(TM) i5-12600K with ASRock Intel Arc B580 Challenger [Alchemist], 12GB:
[...]
The commit is found not by a git bisect (since it's reported by end user and I cannot reproduce it on my hardware) but (by analyzing dmesg) with:
[...]
Then finding the suspecting commit:
Quoted 7 lines
  $ git log --oneline -G'XE_LUNARLAKE' v6.12.74..v6.12.75
  26a40327c25c drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt
6.18 and above are not affected by the bug. Also, they have another commit modifying the line which is not present in 6.12 branch:
[...]
Related drm/xe bug report https://gitlab.freedesktop.org/drm/xe/kernel/-/work_items/7661
Nobody reacted to this and it seems the gitlab ticket is stalled, too. So let me ask: can this be resolved by reverting 26a40327c25c in 6.12.y?

It's turned out these two commits are revertible together:

8f6848b2f6ea ("drm/xe/mmio: Avoid double-adjust in 64-bit reads") 26a40327c25c ("drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt")

I am going to ask the users to test this.

Thanks,

Quoted 28 lines

As of me, this is not easy to revert, as it depends on many other commits, and git does not have tooling to determine all dependant commits for revert. I hope someone from drm subsystem notices this to work on it, or Sasha can pull missing commits or revert this (obviously, he have tooling for this, but I was unable to find it). [I found obsolete references to deps but is seems not used for years and Python git-deps tool seems broken.]
What I found is, offending commit is picked due to
Stable-dep-of: 4a9b4e1fa52a ("drm/xe/mmio: Avoid double-adjust in 64-bit reads")
Which, perhaps, needs to be reverted.
Offending commit 26a40327c25c is not tracked in lore.
It's part of 9 piece patchset, perhaps they are logically dependent too, so need to be reverted together.
The possible fix is part of 6 piece patchset, which does not cherry-pick easily due to conflicts.
If someone can produce correct fix we can participate in the tests.
Thanks,
Quoted 2 lines
Ciao, Thorsten

Vitaly Chikunov

2026-04-14 13:57 UTC #6 lore raw

Thorsten, Sasha,

Quoted 39 lines · Vitaly Chikunov

Quoted 31 lines · Vitaly Chikunov
Quoted 30 lines · Thorsten Leemhuis
Quoted 29 lines · Vitaly Chikunov
1. I cannot find this commit posted on lore.kernel.org to report to exact patch.
| From: Matt Roper <[email protected]>
| Date: Tue, 10 Sep 2024 16:47:29 -0700
| Subject: [PATCH 6.12/sisyphus] drm/xe: Switch MMIO interface to take xe_mmio
|  instead of xe_gt
| 
| [ Upstream commit a84590c5ceb354d2e9f7f6812cfb3a9709e14afa ]
| 
| Since much of the MMIO register access done by the driver is to non-GT
| registers, use of 'xe_gt' in these interfaces has been a long-standing
| design flaw that's been hard to disentangle.
[...]
2. After this patch applied to 6.12.75 there is kernel NULL pointer dereference BUG on MSI MAG H670 12th Gen Intel(R) Core(TM) i5-12600K with ASRock Intel Arc B580 Challenger [Alchemist], 12GB:
[...]
The commit is found not by a git bisect (since it's reported by end user and I cannot reproduce it on my hardware) but (by analyzing dmesg) with:
[...]
Then finding the suspecting commit:
  $ git log --oneline -G'XE_LUNARLAKE' v6.12.74..v6.12.75
  26a40327c25c drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt
Quoted 6 lines
Quoted 6 lines
Quoted 4 lines
6.18 and above are not affected by the bug. Also, they have another commit modifying the line which is not present in 6.12 branch:
[...]
Related drm/xe bug report https://gitlab.freedesktop.org/drm/xe/kernel/-/work_items/7661
Nobody reacted to this and it seems the gitlab ticket is stalled, too. So let me ask: can this be resolved by reverting 26a40327c25c in 6.12.y?

Quoted 6 lines

It's turned out these two commits are revertible together:
8f6848b2f6ea ("drm/xe/mmio: Avoid double-adjust in 64-bit reads") 26a40327c25c ("drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt")
I am going to ask the users to test this.

After testing revert of these two commits, users report that regress does not appear, kernel boots without panic and there is no video artifacts.

So, I kindly ask to revert them from 6.12.y branch if they aren't critical.

Thanks,

Quoted 31 lines

Thanks,
Quoted 28 lines
As of me, this is not easy to revert, as it depends on many other commits, and git does not have tooling to determine all dependant commits for revert. I hope someone from drm subsystem notices this to work on it, or Sasha can pull missing commits or revert this (obviously, he have tooling for this, but I was unable to find it). [I found obsolete references to deps but is seems not used for years and Python git-deps tool seems broken.]
What I found is, offending commit is picked due to
Stable-dep-of: 4a9b4e1fa52a ("drm/xe/mmio: Avoid double-adjust in 64-bit reads")
Which, perhaps, needs to be reverted.
Offending commit 26a40327c25c is not tracked in lore.
It's part of 9 piece patchset, perhaps they are logically dependent too, so need to be reverted together.
The possible fix is part of 6 piece patchset, which does not cherry-pick easily due to conflicts.
If someone can produce correct fix we can participate in the tests.
Thanks,
Quoted 2 lines
Ciao, Thorsten

Vitaly Chikunov

2026-04-14 15:24 UTC #7 lore raw

Thorsten, Sasha,

Quoted 42 lines · Vitaly Chikunov

Quoted 41 lines · Vitaly Chikunov
Quoted 31 lines · Vitaly Chikunov
Quoted 30 lines · Thorsten Leemhuis
Quoted 29 lines · Vitaly Chikunov
1. I cannot find this commit posted on lore.kernel.org to report to exact patch.
| From: Matt Roper <[email protected]>
| Date: Tue, 10 Sep 2024 16:47:29 -0700
| Subject: [PATCH 6.12/sisyphus] drm/xe: Switch MMIO interface to take xe_mmio
|  instead of xe_gt
| 
| [ Upstream commit a84590c5ceb354d2e9f7f6812cfb3a9709e14afa ]
| 
| Since much of the MMIO register access done by the driver is to non-GT
| registers, use of 'xe_gt' in these interfaces has been a long-standing
| design flaw that's been hard to disentangle.
[...]
2. After this patch applied to 6.12.75 there is kernel NULL pointer dereference BUG on MSI MAG H670 12th Gen Intel(R) Core(TM) i5-12600K with ASRock Intel Arc B580 Challenger [Alchemist], 12GB:
[...]
The commit is found not by a git bisect (since it's reported by end user and I cannot reproduce it on my hardware) but (by analyzing dmesg) with:
[...]
Then finding the suspecting commit:
  $ git log --oneline -G'XE_LUNARLAKE' v6.12.74..v6.12.75
  26a40327c25c drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt
Quoted 6 lines
Quoted 6 lines
Quoted 4 lines
6.18 and above are not affected by the bug. Also, they have another commit modifying the line which is not present in 6.12 branch:
[...]
Related drm/xe bug report https://gitlab.freedesktop.org/drm/xe/kernel/-/work_items/7661
Nobody reacted to this and it seems the gitlab ticket is stalled, too. So let me ask: can this be resolved by reverting 26a40327c25c in 6.12.y?
It's turned out these two commits are revertible together:

Quoted 7 lines

Quoted 4 lines
8f6848b2f6ea ("drm/xe/mmio: Avoid double-adjust in 64-bit reads") 26a40327c25c ("drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt")
I am going to ask the users to test this.
After testing revert of these two commits, users report that regress does not appear, kernel boots without panic and there is no video artifacts.

After analyzing the problem slightly deeper, it seems that there is uninitialized mmio.tile issue. Which is fixed in mainline commit

58548b91101f ("drm/xe: Defer gt->mmio initialization until after multi-tile setup")

The commit also have tag:

Fixes fa599b8c95a7 ("drm/xe: Populate GT's mmio iomap from tile during init")

The commit fa599b8c95a7 is picked into 6.12.75 as 0b433e086b9f, but the fix is not. Piking it may be the better way to fix the regression than the revert of the two aforementioned commits.

I will try to pick the fix, test, and report if it resolves the regress.

Thanks,

Quoted 37 lines

So, I kindly ask to revert them from 6.12.y branch if they aren't critical.
Thanks,
Quoted 31 lines
Thanks,
Quoted 28 lines
As of me, this is not easy to revert, as it depends on many other commits, and git does not have tooling to determine all dependant commits for revert. I hope someone from drm subsystem notices this to work on it, or Sasha can pull missing commits or revert this (obviously, he have tooling for this, but I was unable to find it). [I found obsolete references to deps but is seems not used for years and Python git-deps tool seems broken.]
What I found is, offending commit is picked due to
Stable-dep-of: 4a9b4e1fa52a ("drm/xe/mmio: Avoid double-adjust in 64-bit reads")
Which, perhaps, needs to be reverted.
Offending commit 26a40327c25c is not tracked in lore.
It's part of 9 piece patchset, perhaps they are logically dependent too, so need to be reverted together.
The possible fix is part of 6 piece patchset, which does not cherry-pick easily due to conflicts.
If someone can produce correct fix we can participate in the tests.
Thanks,
Quoted 2 lines
Ciao, Thorsten

Vitaly Chikunov

2026-04-15 12:24 UTC #8 lore raw

Thorsten, Sasha,

Quoted 48 lines · Vitaly Chikunov

Quoted 47 lines · Vitaly Chikunov
Quoted 45 lines · Vitaly Chikunov
Quoted 31 lines · Vitaly Chikunov
Quoted 30 lines · Thorsten Leemhuis
Quoted 29 lines · Vitaly Chikunov
1. I cannot find this commit posted on lore.kernel.org to report to exact patch.
| From: Matt Roper <[email protected]>
| Date: Tue, 10 Sep 2024 16:47:29 -0700
| Subject: [PATCH 6.12/sisyphus] drm/xe: Switch MMIO interface to take xe_mmio
|  instead of xe_gt
| 
| [ Upstream commit a84590c5ceb354d2e9f7f6812cfb3a9709e14afa ]
| 
| Since much of the MMIO register access done by the driver is to non-GT
| registers, use of 'xe_gt' in these interfaces has been a long-standing
| design flaw that's been hard to disentangle.
[...]
2. After this patch applied to 6.12.75 there is kernel NULL pointer dereference BUG on MSI MAG H670 12th Gen Intel(R) Core(TM) i5-12600K with ASRock Intel Arc B580 Challenger [Alchemist], 12GB:
[...]
The commit is found not by a git bisect (since it's reported by end user and I cannot reproduce it on my hardware) but (by analyzing dmesg) with:
[...]
Then finding the suspecting commit:
  $ git log --oneline -G'XE_LUNARLAKE' v6.12.74..v6.12.75
  26a40327c25c drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt
Quoted 6 lines
Quoted 6 lines
Quoted 4 lines
6.18 and above are not affected by the bug. Also, they have another commit modifying the line which is not present in 6.12 branch:
[...]
Related drm/xe bug report https://gitlab.freedesktop.org/drm/xe/kernel/-/work_items/7661
Nobody reacted to this and it seems the gitlab ticket is stalled, too. So let me ask: can this be resolved by reverting 26a40327c25c in 6.12.y?
It's turned out these two commits are revertible together:
8f6848b2f6ea ("drm/xe/mmio: Avoid double-adjust in 64-bit reads") 26a40327c25c ("drm/xe: Switch MMIO interface to take xe_mmio instead of xe_gt")
I am going to ask the users to test this.

Quoted 7 lines

Quoted 2 lines
After testing revert of these two commits, users report that regress does not appear, kernel boots without panic and there is no video artifacts.
After analyzing the problem slightly deeper, it seems that there is uninitialized mmio.tile issue. Which is fixed in mainline commit
58548b91101f ("drm/xe: Defer gt->mmio initialization until after multi-tile setup")

Applying this commit to v6.12.81 does not resolve the regress. Thus, I would suggest reverting commits 26a40327c25c and 8f6848b2f6ea.

Thanks,

Quoted 51 lines

The commit also have tag:
Fixes fa599b8c95a7 ("drm/xe: Populate GT's mmio iomap from tile during init")
The commit fa599b8c95a7 is picked into 6.12.75 as 0b433e086b9f, but the fix is not. Piking it may be the better way to fix the regression than the revert of the two aforementioned commits.
I will try to pick the fix, test, and report if it resolves the regress.
Thanks,
Quoted 37 lines
So, I kindly ask to revert them from 6.12.y branch if they aren't critical.
Thanks,
Quoted 31 lines
Thanks,
Quoted 28 lines
As of me, this is not easy to revert, as it depends on many other commits, and git does not have tooling to determine all dependant commits for revert. I hope someone from drm subsystem notices this to work on it, or Sasha can pull missing commits or revert this (obviously, he have tooling for this, but I was unable to find it). [I found obsolete references to deps but is seems not used for years and Python git-deps tool seems broken.]
What I found is, offending commit is picked due to
Stable-dep-of: 4a9b4e1fa52a ("drm/xe/mmio: Avoid double-adjust in 64-bit reads")
Which, perhaps, needs to be reverted.
Offending commit 26a40327c25c is not tracked in lore.
It's part of 9 piece patchset, perhaps they are logically dependent too, so need to be reverted together.
The possible fix is part of 6 piece patchset, which does not cherry-pick easily due to conflicts.
If someone can produce correct fix we can participate in the tests.
Thanks,
Quoted 2 lines
Ciao, Thorsten