/freebsd-src/sys/contrib/device-tree/Bindings/interrupt-controller/ |
H A D | ti,sci-intr.yaml | 1 # SPDX-License-Identifier: (GPL-2.0 OR BSD-2-Clause) 3 --- 4 $id: http://devicetree.org/schemas/interrupt-controller/ti,sci-intr.yaml# 5 $schema: http://devicetree.org/meta-schemas/core.yaml# 10 - Lokesh Vutla <lokeshvutla@ti.com> 13 - $ref: /schemas/arm/keystone/ti,k3-sci-common.yaml# 16 The Interrupt Router (INTR) module provides a mechanism to mux M 22 +----------------------+ 24 +-------+ | +------+ +-----+ | 25 | GPIO |----------->| | irq0 | | 0 | | Host IRQ [all …]
|
H A D | ti,sci-intr.txt | 4 The Interrupt Router (INTR) module provides a mechanism to mux M 10 +----------------------+ 12 +-------+ | +------+ +-----+ | 13 | GPIO |----------->| | irq0 | | 0 | | Host IRQ 14 +-------+ | +------+ +-----+ | controller 15 | . . | +-------+ 16 +-------+ | . . |----->| IRQ | 17 | INTA |----------->| . . | +-------+ 18 +-------+ | . +-----+ | 19 | +------+ | N | | [all …]
|
/freebsd-src/sys/x86/acpica/ |
H A D | madt.c | 1 /*- 2 * SPDX-License-Identifier: BSD-2-Clause 72 static int madt_find_interrupt(int intr, void **apic, u_int *pin); 75 ACPI_MADT_INTERRUPT_OVERRIDE *intr); 109 return (-50); in madt_probe() 120 madt_length = madt->Header.Length; in madt_probe_cpus() 121 KASSERT(madt != NULL, ("Unable to re-map MADT")); in madt_probe_cpus() 154 if ((dmartbl->Flags & ACPI_DMAR_X2APIC_OPT_OUT) != 0) in madt_x2apic_disable_reason() 166 return ("inside VMWare without intr redirection"); in madt_x2apic_disable_reason() 174 * It seems that some SandyBridge-based notebook in madt_x2apic_disable_reason() [all …]
|
/freebsd-src/sys/arm/arm/ |
H A D | pmu_acpi.c | 1 /*- 2 * SPDX-License-Identifier: BSD-2-Clause 50 ACPI_MADT_GENERIC_INTERRUPT *intr; in madt_handler() local 61 sc = ctx->sc; in madt_handler() 62 rid = ctx->i; in madt_handler() 63 cpuid = -1; in madt_handler() 65 if (ctx->error) in madt_handler() 68 if (entry->Type != ACPI_MADT_TYPE_GENERIC_INTERRUPT) in madt_handler() 70 intr = (ACPI_MADT_GENERIC_INTERRUPT *)entry; in madt_handler() 74 if (pcpu != NULL && PCPU_GET_MPIDR(pcpu) == intr->ArmMpidr) { in madt_handler() [all …]
|
H A D | gic.c | 1 /*- 2 * SPDX-License-Identifier: BSD-3-Clause 61 #include <machine/intr.h> 104 ((_sc->typer & GICD_TYPER_SECURITYEXT) == GICD_TYPER_SECURITYEXT) 117 /* be used for MSI/MSI-X interrupts */ 119 /* for a MSI/MSI-X interrupt */ 127 static u_int sgi_to_ipi[GIC_LAST_SGI - GIC_FIRST_SG 439 arm_gic_alloc_resource(device_t bus,device_t child,int type,int * rid,rman_res_t start,rman_res_t end,rman_res_t count,u_int flags) arm_gic_alloc_resource() argument [all...] |
/freebsd-src/sys/dev/spibus/controller/allwinner/ |
H A D | aw_spi.c | 1 /*- 61 #define AW_SPI_TCR_DDB (1 << 9) /* Dummy Burst Type */ 88 #define AW_SPI_FCR_TX_TRIG_MASK 0xFF0000 /* TX FIFO Trigger level */ 91 #define AW_SPI_FCR_RX_TRIG_MASK 0xFF /* RX FIFO Trigger level */ 126 { "allwinner,sun8i-h3-spi", 1 }, 133 { -1, 0 } 156 #define AW_SPI_LOCK(sc) mtx_lock(&(sc)->mtx) 157 #define AW_SPI_UNLOCK(sc) mtx_unlock(&(sc)->mtx) 158 #define AW_SPI_ASSERT_LOCKED(sc) mtx_assert(&(sc)->mt 426 uint32_t intr; aw_spi_intr() local [all...] |
/freebsd-src/sys/contrib/device-tree/src/arm64/ti/ |
H A D | k3-am65-wakeup.dtsi | 1 // SPDX-License-Identifier: GPL-2.0-only OR MIT 5 * Copyright (C) 2016-2024 Texas Instruments Incorporated - https://www.ti.com/ 9 dmsc: system-controller@44083000 { 10 compatible = "ti,am654-sci"; 11 ti,host-id = <12>; 13 mbox-name [all...] |
H A D | k3-am64-mcu.dtsi | 1 // SPDX-License-Identifier: GPL-2.0-only OR MIT 5 * Copyright (C) 2020-2024 Texas Instruments Incorporated - https://www.ti.com/ 15 compatible = "ti,am654-timer"; 18 clock-names = "fck"; 19 power-domains = <&k3_pds 35 TI_SCI_PD_EXCLUSIVE>; 20 ti,timer-pw [all...] |
H A D | k3-am62a-mcu.dtsi | 1 // SPDX-License-Identifier: GPL-2.0-only OR MIT 5 * Copyright (C) 2020-2024 Texas Instruments Incorporated - https://www.ti.com/ 10 compatible = "pinctrl-single"; 12 #pinctrl-cells = <1>; 13 pinctrl-single,register-widt [all...] |
H A D | k3-am62-mcu.dtsi | 1 // SPDX-License-Identifier: GPL-2.0-only OR MIT 5 * Copyright (C) 2020-2024 Texas Instruments Incorporated - https://www.ti.com/ 10 bootph-all; 11 compatible = "pinctrl-single"; 13 #pinctrl-cells = <1>; 14 pinctrl-singl [all...] |
H A D | k3-am62p-mcu.dtsi | 1 // SPDX-License-Identifier: GPL-2.0-only OR MIT 4 * Copyright (C) 2023-2024 Texas Instruments Incorporated - https://www.ti.com/ 9 compatible = "pinctrl-single"; 11 #pinctrl-cells = <1>; 12 pinctrl-single,register-widt [all...] |
H A D | k3-j721e-mcu-wakeup.dtsi | 1 // SPDX-License-Identifier: GPL-2.0-only OR MIT 5 * Copyright (C) 2016-2024 Texas Instruments Incorporated - https://www.ti.com/ 9 dmsc: system-controller@44083000 { 10 compatible = "ti,k2g-sci"; 11 ti,host-id = <12>; 13 mbox-name [all...] |
H A D | k3-j7200-mcu-wakeup.dtsi | 1 // SPDX-License-Identifier: GPL-2.0-only OR MIT 5 * Copyright (C) 2020-2024 Texas Instruments Incorporated - https://www.ti.com/ 9 dmsc: system-controller@44083000 { 10 compatible = "ti,k2g-sci"; 11 ti,host-id = <12>; 13 mbox-name [all...] |
H A D | k3-j784s4-mcu-wakeup.dtsi | 1 // SPDX-License-Identifier: GPL-2.0-only OR MIT 5 * Copyright (C) 2022-2024 Texas Instruments Incorporated - https://www.ti.com/ 9 sms: system-controller@44083000 { 10 bootph-all; 11 compatible = "ti,k2g-sci"; 12 ti,host-i [all...] |
H A D | k3-j721s2-mcu-wakeup.dtsi | 1 // SPDX-License-Identifier: GPL-2.0-only OR MIT 5 * Copyright (C) 2021-2024 Texas Instruments Incorporated - https://www.ti.com/ 9 sms: system-controller@44083000 { 10 compatible = "ti,k2g-sci"; 11 ti,host-id = <12>; 13 mbox-name [all...] |
/freebsd-src/sys/arm/allwinner/ |
H A D | aw_nmi.c | 1 /*- 37 #include <machine/intr.h> 61 #define SC_NMI_READ(_sc, _reg) bus_read_4(_sc->res[0], _reg) 62 #define SC_NMI_WRITE(_sc, _reg, _val) bus_write_4(_sc->res[0], _reg, _val) 67 { -1, 0, 0 } 87 struct aw_nmi_intr intr; member 110 {"allwinner,sun7i-a20-sc-nmi", (uintptr_t)&a20_nmi_cfg}, 111 {"allwinner,sun6i-a31-sc-nmi", (uintptr_t)&a31_nmi_cfg}, 112 {"allwinner,sun6i-a31-r-intc", (uintptr_t)&a83t_r_nmi_cfg}, 113 {"allwinner,sun8i-a83t-r-intc", (uintptr_t)&a83t_r_nmi_cfg}, [all …]
|
/freebsd-src/tools/test/gpioevents/ |
H A D | gpioevents.c | 1 /*- 2 * SPDX-License-Identifier: BSD-2-Clause 28 * make LDFLAGS+=-lgpio gpioevents 66 fprintf(stderr, "usage: %s [-f ctldev] [-m method] [-s] [-n] [-S] [-u]" in usage() 67 "[-t timeout] [-d delay-usec] pin intr-config pin-mode [pin intr-config pin-mode ...]\n\n", in usage() 69 fprintf(stderr, " -d delay before each call to read/poll/select/etc\n"); in usage() 70 fprintf(stderr, " -n Non-blocking IO\n"); in usage() 71 fprintf(stderr, " -s Single-shot (else loop continuously)\n"); in usage() 72 fprintf(stderr, " -S Report summary data (else report each event)\n"); in usage() 73 fprintf(stderr, " -u Show timestamps as UTC (else monotonic time)\n"); in usage() [all …]
|
/freebsd-src/sys/x86/x86/ |
H A D | mptable.c | 1 /*- 2 * SPDX-License-Identifier: BSD-2-Clause 76 uint8_t type; 106 u_char type; 110 /* From MP spec v1.4, table 4-8. */ 133 /* From MP spec v1.4, table 5-1. */ 163 static int pci0 = - 82 uint8_t type; global() member 112 u_char type; global() member 734 intentry_polarity(int_entry_ptr intr) intentry_polarity() argument 751 intentry_trigger(int_entry_ptr intr) intentry_trigger() argument 771 mptable_parse_io_int(int_entry_ptr intr) mptable_parse_io_int() argument 862 mptable_parse_local_int(int_entry_ptr intr) mptable_parse_local_int() argument 913 int_entry_ptr intr; mptable_parse_ints_handler() local 1082 int_entry_ptr intr; mptable_pci_probe_table_handler() local 1118 int_entry_ptr intr; mptable_pci_route_interrupt_handler() local 1201 int error, *flagp, flags, type; mptable_host_res_handler() local [all...] |
/freebsd-src/sys/arm/ti/ |
H A D | ti_sdma.c | 1 /*- 2 * SPDX-License-Identifier: BSD-2-Clause 44 #include <machine/intr.h> 133 #define TI_SDMA_LOCK(_sc) mtx_lock_spin(&(_sc)->sc_mtx) 134 #define TI_SDMA_UNLOCK(_sc) mtx_unlock_spin(&(_sc)->sc_mtx) 136 mtx_init(&_sc->sc_mtx, device_get_nameunit(_sc->sc_dev), \ 138 #define TI_SDMA_LOCK_DESTROY(_sc) mtx_destroy(&_sc->sc_mtx); 139 #define TI_SDMA_ASSERT_LOCKED(_sc) mtx_assert(&_sc->sc_mtx, MA_OWNED); 140 #define TI_SDMA_ASSERT_UNLOCKED(_sc) mtx_assert(&_sc->sc_mtx, MA_NOTOWNED); 149 * ti_sdma_read_4 - reads a 32-bit value from one of the DMA registers [all …]
|
/freebsd-src/contrib/llvm-project/clang/utils/TableGen/ |
H A D | NeonEmitter.cpp | 1 //===- NeonEmitter.cpp - Generate arm_neon.h for use with clang -*- C++ -*-===// 5 // SPDX-License-Identifier: Apache-2.0 WITH LLVM-exceptio 140 class Type { global() class 161 Type() Type() function in __anonabaaf6210111::Type 166 Type(TypeSpec TS, StringRef CharMods) Type() function in __anonabaaf6210111::Type 392 for (const auto &Type : Types) { Intrinsic() local 518 Intrinsic &Intr; global() member in __anonabaaf6210111::Intrinsic::DagEmitter 522 DagEmitter(Intrinsic & Intr,StringRef CallPrefix) DagEmitter() argument 1938 __anonabaaf6210502(const auto &Type) getIntrinsic() argument 2104 const auto &Type = Def->getParamType(I); genOverloadTypeCheckCode() local [all...] |
/freebsd-src/sys/kern/ |
H A D | subr_kdb.c | 1 /*- 2 * SPDX-License-Identifier: BSD-2-Clause 119 "trigger a kernel panic, using the provided string as the panic message"); 163 if ((*iter)->dbbe_active == 0) in kdb_sysctl_available() 164 sbuf_printf(&sbuf, "%s ", (*iter)->dbbe_name); in kdb_sysctl_available() 178 strlcpy(buf, kdb_dbbe->dbbe_name, sizeof(buf)); in kdb_sysctl_current() 182 if (error != 0 || req->newpt in kdb_sysctl_current() 740 kdb_trap(int type,int code,struct trapframe * tf) kdb_trap() argument 746 register_t intr; kdb_trap() local [all...] |
/freebsd-src/sys/dev/enic/ |
H A D | vnic_devcmd.h | 1 /* SPDX-License-Identifier: BSD-3-Clause 2 * Copyright 2008-2017 Cisco Systems, Inc. All rights reserved. 14 #define _CMD_NMASK ((1 << _CMD_NBITS)-1) 15 #define _CMD_VTYPEMASK ((1 << _CMD_VTYPEBITS)-1) 16 #define _CMD_FLAGSMASK ((1 << _CMD_FLAGSBITS)-1) 17 #define _CMD_DIRMASK ((1 << _CMD_DIRBITS)-1) 39 * vNIC type bits. 100 /* dev-specific block member: 179 * (u16)a1 & 0x0000ffff00000000=intr num (-1 for no intr) 271 * a2-a15=args to cmd in a1 [all …]
|
/freebsd-src/sys/dts/arm/ |
H A D | annapurna-alpine.dts | 1 /*- 28 /dts-v1/; 32 #address-cells = <1>; 33 #size-cells = <1>; 40 #address-cells = <1>; 41 #size-cells = <0>; 45 compatible = "arm,cortex-a15"; 47 d-cache-line-size = <64>; // 64 bytes 48 i-cache-line-size = <64>; // 64 bytes 49 d-cache-size = <0x8000>; // L1, 32K [all …]
|
/freebsd-src/sys/dev/sound/pci/ |
H A D | envy24ht.c | 1 /*- 2 * SPDX-License-Identifier: BSD-2-Clause 35 * generous gift - an 'Audiotrak Prodigy HD2' audio card! I also want to 58 /* ---- 121 u_int8_t cif, type, free; global() member 170 u_int16_t intr[2]; global() member 1158 u_int32_t mask, intr; envy24ht_updintr() local 1198 u_int32_t mask, intr; envy24ht_maskintr() local 1217 u_int32_t mask, stat, intr, rtn; envy24ht_checkintr() local [all...] |
/freebsd-src/sys/contrib/device-tree/src/powerpc/ |
H A D | mpc8379_rdb.dts | 1 // SPDX-License-Identifier: GPL-2.0-or-later 8 /dts-v1/; 12 #address-cells = <1>; 13 #size-cells = <1>; 24 #address-cells = <1>; 25 #size-cells = <0>; 30 d-cache-line-size = <32>; 31 i-cache-line-size = <32>; 32 d-cache-size = <32768>; 33 i-cache-size = <32768>; [all …]
|