Home
last modified time | relevance | path

Searched +full:intr +full:- +full:trigger +full:- +full:type (Results 1 – 25 of 76) sorted by relevance

1234

/freebsd-src/sys/contrib/device-tree/Bindings/interrupt-controller/
H A Dti,sci-intr.yaml1 # 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 Dti,sci-intr.txt4 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 Dmadt.c1 /*-
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 Dpmu_acpi.c1 /*-
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 Dgic.c1 /*-
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 Daw_spi.c1 /*-
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 Dk3-am65-wakeup.dtsi1 // 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 Dk3-am64-mcu.dtsi1 // 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 Dk3-am62a-mcu.dtsi1 // 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 Dk3-am62-mcu.dtsi1 // 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 Dk3-am62p-mcu.dtsi1 // 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 Dk3-j721e-mcu-wakeup.dtsi1 // 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 Dk3-j7200-mcu-wakeup.dtsi1 // 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 Dk3-j784s4-mcu-wakeup.dtsi1 // 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 Dk3-j721s2-mcu-wakeup.dtsi1 // 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 Daw_nmi.c1 /*-
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 Dgpioevents.c1 /*-
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 Dmptable.c1 /*-
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 Dti_sdma.c1 /*-
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 DNeonEmitter.cpp1 //===- 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 Dsubr_kdb.c1 /*-
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 Dvnic_devcmd.h1 /* 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 Dannapurna-alpine.dts1 /*-
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 Denvy24ht.c1 /*-
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 Dmpc8379_rdb.dts1 // 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 …]

1234