Home
last modified time | relevance | path

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

1234

/freebsd/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/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/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_SGI + 1];
131 #define GIC_INTR_ISRC(sc, irq) (&sc->gic_irqs[irq].gi_isrc)
137 { -1, 0 }
153 bus_read_4((_sc)->gic_res[GIC_RES_CPU], (_reg))
[all …]
/freebsd/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)->mtx, MA_OWNED)
159 #define AW_SPI_READ_1(sc, reg) bus_read_1((sc)->res[0], (reg))
[all …]
/freebsd/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/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/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-names = "rx", "tx";
18 reg-names = "debug_messages";
21 k3_pds: power-controller {
22 compatible = "ti,sci-pm-domain";
23 #power-domain-cells = <2>;
[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-pwm;
25 compatible = "ti,am654-timer";
28 clock-names = "fck";
29 power-domains = <&k3_pds 48 TI_SCI_PD_EXCLUSIVE>;
30 ti,timer-pwm;
[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-single,register-width = <32>;
15 pinctrl-single,function-mask = <0xffffffff>;
19 bootph-pre-ram;
20 compatible = "ti,j721e-esm";
23 ti,esm-pins = <0>, <1>, <2>, <85>;
[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-width = <32>;
14 pinctrl-single,function-mask = <0xffffffff>;
19 compatible = "ti,j721e-esm";
21 bootph-pre-ram;
23 ti,esm-pins = <0>, <1>, <2>, <85>;
32 compatible = "ti,am654-timer";
[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-width = <32>;
13 pinctrl-single,function-mask = <0xffffffff>;
14 bootph-all;
18 compatible = "ti,j721e-esm";
20 ti,esm-pins = <0>, <1>, <2>, <85>;
22 bootph-pre-ram;
[all …]
H A Dk3-am62p-j722s-common-mcu.dtsi1 // SPDX-License-Identifier: GPL-2.0-only OR MIT
5 * Copyright (C) 2023-2024 Texas Instruments Incorporated - https://www.ti.com/
10 compatible = "pinctrl-single";
12 #pinctrl-cells = <1>;
13 pinctrl-single,register-width = <32>;
14 pinctrl-single,function-mask = <0xffffffff>;
15 pinctrl-single,gpio-range =
19 bootph-all;
21 mcu_pmx_range: gpio-range {
22 #pinctrl-single,gpio-range-cells = <3>;
[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-names = "rx", "tx";
18 reg-names = "debug_messages";
21 k3_pds: power-controller {
22 compatible = "ti,sci-pm-domain";
23 #power-domain-cells = <2>;
[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-id = <12>;
14 mbox-names = "rx", "tx";
19 reg-names = "debug_messages";
22 k3_pds: power-controller {
23 bootph-all;
[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-names = "rx", "tx";
18 reg-names = "debug_messages";
21 k3_pds: power-controller {
22 compatible = "ti,sci-pm-domain";
23 #power-domain-cells = <2>;
[all …]
/freebsd/sys/x86/x86/
H A Dmptable.c1 /*-
2 * SPDX-License-Identifier: BSD-2-Clause
76 uint8_t type; member
106 u_char type; member
110 /* From MP spec v1.4, table 4-8. */
133 /* From MP spec v1.4, table 5-1. */
163 static int pci0 = -1;
170 static enum intr_polarity intentry_polarity(int_entry_ptr intr);
171 static enum intr_trigger intentry_trigger(int_entry_ptr intr);
184 static void mptable_parse_io_int(int_entry_ptr intr);
[all …]
/freebsd/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/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-exception
7 //===----------------------------------------------------------------------===//
14 // are suffixed with the element type of the input vectors. Functions may be
15 // implemented in terms of generic vector operations such as +, *, -, etc. or
16 // by calling a __builtin_-prefixed function which will be handled by clang's
24 //===----------------------------------------------------------------------===//
64 PrintFatalError(CurrentRecord->getLoc(), Str); in assert_with_loc()
74 ClassW, // width-specific instruction, e.g., "8" suffix
75 ClassB, // bitcast arguments with enum argument to specify type
[all …]
/freebsd/sys/riscv/riscv/
H A Dplic.c1 /*-
2 * SPDX-License-Identifier: BSD-2-Clause
10 * and Technology) under DARPA contract HR0011-18-C-0016 ("ECATS"), as part of
46 #include <machine/intr.h>
52 #include <dt-bindings/interrupt-controller/irq.h>
70 (_sc->contexts[_cpu].enable_offset + ((_irq) / 32) * sizeof(uint32_t))
72 (_sc->contexts[_cpu].context_offset + PLIC_CONTEXT_THRESHOLD)
74 (_sc->contexts[_cpu].context_offset + PLIC_CONTEXT_CLAIM)
107 { "sifive,plic-1.0.0", 1 },
108 { "thead,c900-plic", 1 },
[all …]
/freebsd/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/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/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/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; member
170 u_int16_t intr[2]; member
178 /* -------------------------------------------------------------------- */
214 /* -------------------------------------------------------------------- */
220 /* API -> hardware channel map */
235 /* mixer -> API channel map. see above */
[all …]

1234