Home
last modified time | relevance | path

Searched +full:4 +full:- +full:pair (Results 1 – 25 of 806) sorted by relevance

12345678910>>...33

/linux/sound/soc/fsl/
H A Dfsl_asrc.c1 // SPDX-License-Identifier: GPL-2.0
11 #include <linux/dma-mapping.h>
14 #include <linux/dma/imx-dma.h>
26 dev_err(&asrc->pdev->dev, "Pair %c: " fmt, 'A' + index, ##__VA_ARGS__)
29 dev_dbg(&asrc->pdev->dev, "Pair %c: " fmt, 'A' + index, ##__VA_ARGS__)
32 dev_warn(&asrc->pdev->dev, "Pair %c: " fmt, 'A' + index, ##__VA_ARGS__)
50 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 0xa, 0xb, 0xc, 0xd, 0xe, 0xf,
56 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 0xa, 0xb, 0xc, 0xd, 0xe, 0xf,
114 1, 2, 4, 8, 16, 32, 64, 128, /* divider = 1 */
115 2, 4, 8, 16, 32, 64, 128, 256, /* divider = 2 */
[all …]
H A Dfsl_asrc_m2m.c1 // SPDX-License-Identifier: GPL-2.0
3 // Copyright (C) 2014-2016 Freescale Semiconductor, Inc.
4 // Copyright (C) 2019-2024 NXP
8 #include <linux/dma/imx-dma.h>
9 #include <linux/dma-buf.h>
10 #include <linux/dma-mapping.h>
33 struct fsl_asrc_pair *pair = (struct fsl_asrc_pair *)data; in asrc_input_dma_callback() local
35 complete(&pair->complete[IN]); in asrc_input_dma_callback()
41 struct fsl_asrc_pair *pair = (struct fsl_asrc_pair *)data; in asrc_output_dma_callback() local
43 complete(&pair->complete[OUT]); in asrc_output_dma_callback()
[all …]
/linux/arch/mips/include/asm/
H A Dmaar.h1 /* SPDX-License-Identifier: GPL-2.0-or-later */
14 * platform_maar_init() - perform platform-level MAAR configuration
18 * MAAR pairs as required, from 0 up to the maximum of num_pairs-1, and returns
28 * write_maar_pair() - write to a pair of MAARs
29 * @idx: The index of the pair (ie. use MAARs idx*2 & (idx*2)+1).
30 * @lower: The lowest address that the MAAR pair will affect. Must be
32 * @upper: The highest address that the MAAR pair will affect. Must be
37 * Program the pair of MAAR registers specified by idx to apply the attributes
43 /* Addresses begin at bit 16, but are shifted right 4 bits */ in write_maar_pair()
44 BUG_ON(lower & (0xffff | ~(MIPS_MAAR_ADDR << 4))); in write_maar_pair()
[all …]
/linux/tools/testing/selftests/riscv/vector/
H A Dv_helpers.c1 // SPDX-License-Identifier: GPL-2.0-only
13 struct riscv_hwprobe pair; in is_xtheadvector_supported() local
15 pair.key = RISCV_HWPROBE_KEY_VENDOR_EXT_THEAD_0; in is_xtheadvector_supported()
16 riscv_hwprobe(&pair, 1, 0, NULL, 0); in is_xtheadvector_supported()
17 return pair.value & RISCV_HWPROBE_VENDOR_EXT_XTHEADVECTOR; in is_xtheadvector_supported()
22 struct riscv_hwprobe pair; in is_vector_supported() local
24 pair.key = RISCV_HWPROBE_KEY_IMA_EXT_0; in is_vector_supported()
25 riscv_hwprobe(&pair, 1, 0, NULL, 0); in is_vector_supported()
26 return pair.value & RISCV_HWPROBE_EXT_ZVE32X; in is_vector_supported()
31 char *exec_argv[4], *exec_envp[1]; in launch_test()
[all …]
/linux/tools/testing/selftests/riscv/hwprobe/
H A Dcbo.c1 // SPDX-License-Identifier: GPL-2.0-only
5 * Run with 'taskset -c <cpu-list> cbo' to only execute hwprobe on a
30 unsigned long *regs = (unsigned long *)&((ucontext_t *)context)->uc_mcontext; in sigill_handler()
36 regs[0] += 4; in sigill_handler()
44 ".4byte %2\n" \
51 static void cbo_zero(char *base) { cbo_insn(base, 4); } in cbo_zero()
85 return n != 0 && (n & (n - 1)) == 0; in is_power_of_2()
90 struct riscv_hwprobe pair = { in test_zicbom() local
97 rc = riscv_hwprobe(&pair, 1, sizeof(cpu_set_t), (unsigned long *)cpus, 0); in test_zicbom()
98 block_size = pair.value; in test_zicbom()
[all …]
/linux/include/linux/
H A Dbrcmphy.h1 /* SPDX-License-Identifier: GPL-2.0 */
7 /* All Broadcom Ethernet switches have a pseudo-PHY at address 30 which is used
94 #define MII_BCM54XX_EXP_SEL_WOL 0x0e00 /* Wake-on-LAN expansion select register */
111 #define MII_BCM54XX_INT_ANPR 0x0400 /* Auto-negotiation page received */
115 #define MII_BCM54XX_INT_PSERR 0x4000 /* Pair swap error */
170 * Broadcom Multicolor LED configurations (expansion register 4)
212 /* 01010: Auto Power-Down */
221 #define BCM54XX_SHD_LEDS_SHIFT(led) (4 * (led))
222 #define BCM54XX_SHD_LEDS1_LED3(src) ((src & 0xf) << 4)
231 /* 10011: SerDes 100-FX Control Register */
[all …]
/linux/drivers/ata/
H A Dpata_ali.c2 * pata_ali.c - ALI 15x3 PATA for new ATA layer
8 * Copyright (C) 1998-2000 Michel Aubry, Maintainer
9 * Copyright (C) 1998-2000 Andrzej Krzysztofowicz, Maintainer
10 * Copyright (C) 1999-2000 CJ, cjtsai@ali.com.tw, Maintainer
12 * Copyright (C) 1998-2000 Andre Hedrick (andre@linux-ide.org)
54 DMI_MATCH(DMI_BOARD_VENDOR, "Hewlett-Packard"),
55 DMI_MATCH(DMI_BOARD_VERSION, "OmniBook N32N-736"),
59 .ident = "Toshiba Satellite S1800-814",
62 DMI_MATCH(DMI_PRODUCT_NAME, "S1800-814"),
71 if (pdev->subsystem_vendor == 0x10CF && pdev->subsystem_device == 0x10AF) in ali_cable_override()
[all …]
H A Dpata_cmd640.c1 // SPDX-License-Identifier: GPL-2.0-only
3 * pata_cmd640.c - CMD640 PCI PATA for new ATA layer
9 * Copyright (C) 1995-1996 Linus Torvalds & authors (see driver)
45 * cmd640_set_piomode - set initial PIO mode data
54 struct cmd640_reg *timing = ap->private_data; in cmd640_set_piomode()
55 struct pci_dev *pdev = to_pci_dev(ap->host->dev); in cmd640_set_piomode()
60 int arttim = ARTIM0 + 2 * adev->devno; in cmd640_set_piomode()
61 struct ata_device *pair = ata_dev_pair(adev); in cmd640_set_piomode() local
63 if (ata_timing_compute(adev, adev->pio_mode, &t, T, 0) < 0) { in cmd640_set_piomode()
70 if (ap->port_no && pair) { in cmd640_set_piomode()
[all …]
/linux/arch/s390/include/asm/
H A Dcpacf.h1 /* SPDX-License-Identifier: GPL-2.0 */
15 #include <linux/kmsan-checks.h>
180 #define CPACF_KMA_LPC 0x100 /* Last-Plaintext/Ciphertext */
181 #define CPACF_KMA_LAAD 0x200 /* Last-AAD */
182 #define CPACF_KMA_HS 0x400 /* Hash-subkey Supplied */
266 __cpacf_query_rre(CPACF_KM, 2, 4, pb, fc); in __cpacf_query_insn()
269 __cpacf_query_rrf(CPACF_KMA, 2, 4, 6, 0, pb, fc); in __cpacf_query_insn()
275 __cpacf_query_rre(CPACF_KMC, 2, 4, pb, fc); in __cpacf_query_insn()
278 __cpacf_query_rrf(CPACF_KMCTR, 2, 4, 6, 0, pb, fc); in __cpacf_query_insn()
281 __cpacf_query_rre(CPACF_KMF, 2, 4, pb, fc); in __cpacf_query_insn()
[all …]
/linux/crypto/
H A Daegis128-neon-inner.c1 // SPDX-License-Identifier: GPL-2.0-or-later
7 #include <asm/neon-intrinsics.h>
19 #include "aegis-neon.h"
48 vst1q_u8(state + 64, st.v[4]); in aegis128_save_state_neon()
74 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0x40), w - 0x40); in aegis_aes_round()
75 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0x80), w - 0x80); in aegis_aes_round()
76 v = vqtbx4q_u8(v, vld1q_u8_x4(crypto_aes_sbox + 0xc0), w - 0xc0); in aegis_aes_round()
78 asm("tbl %0.16b, {v16.16b-v19.16b}, %1.16b" : "=w"(v) : "w"(w)); in aegis_aes_round()
79 w -= 0x40; in aegis_aes_round()
80 asm("tbx %0.16b, {v20.16b-v23.16b}, %1.16b" : "+w"(v) : "w"(w)); in aegis_aes_round()
[all …]
/linux/tools/perf/tests/
H A Dvmlinux-kallsyms.c1 // SPDX-License-Identifier: GPL-2.0
26 * when --all-symbols is specified so exclude them to get a in is_ignored_symbol()
48 "__kvm_nvhe_$", /* arm64 local symbols in non-VHE KVM namespace */ in is_ignored_symbol()
49 "__kvm_nvhe_.L", /* arm64 local symbols in non-VHE KVM namespace */ in is_ignored_symbol()
85 int l = strlen(name) - strlen(*p); in is_ignored_symbol()
130 struct map *pair = maps__find_by_name(args->kallsyms.kmaps, in test__vmlinux_matches_kallsyms_cb1() local
133 if (pair) { in test__vmlinux_matches_kallsyms_cb1()
134 map__set_priv(pair); in test__vmlinux_matches_kallsyms_cb1()
135 map__put(pair); in test__vmlinux_matches_kallsyms_cb1()
137 if (!args->header_printed) { in test__vmlinux_matches_kallsyms_cb1()
[all …]
/linux/Documentation/networking/pse-pd/
H A Dintroduction.rst1 .. SPDX-License-Identifier: GPL-2.0
7 --------
15 ----------------
22 with single balanced twisted-pair PHYs, as per Clause 104 of IEEE 802.3. PoDL
24 and data delivery over a single pair is advantageous.
26 IEEE 802.3-2018 Addendums and Related Clauses
27 ---------------------------------------------
29 Key addenda to the IEEE 802.3-2018 standard relevant to power delivery over
32 - **802.3af (Approved in 2003-06-12)**: Known as PoE in the market, detailed in
34 - **802.3at (Approved in 2009-09-11)**: Marketed as PoE+, enhancing PoE as
[all …]
H A Dpse-pi.rst1 .. SPDX-License-Identifier: GPL-2.0
9 eight-pin modular jack, commonly known as the Ethernet RJ45 port. This
14 ---------------------------
19 - Section "33.2.3 PI pin assignments" covers the pin assignments for PoE
21 - Section "145.2.4 PSE PI" addresses the configuration for PoE systems that
24 PSE PI and Single Pair Ethernet
25 -------------------------------
27 Single Pair Ethernet (SPE) represents a different approach to Ethernet
28 connectivity, utilizing just one pair of conductors for both data and power
31 two pairs of wires, SPE operates on a simpler model due to its single-pair
[all …]
/linux/samples/bpf/
H A Dsockex2_kern.c39 return 4; in proto_ports_offset()
54 __u64 w1 = load_word(ctx, off + 4); in ipv6_addr_hash()
72 flow->src = load_word(skb, nhoff + offsetof(struct iphdr, saddr)); in parse_ip()
73 flow->dst = load_word(skb, nhoff + offsetof(struct iphdr, daddr)); in parse_ip()
90 flow->src = ipv6_addr_hash(skb, in parse_ipv6()
92 flow->dst = ipv6_addr_hash(skb, in parse_ipv6()
142 nhoff += 4; in flow_dissector()
144 nhoff += 4; in flow_dissector()
146 nhoff += 4; in flow_dissector()
148 nhoff += 4; in flow_dissector()
188 struct pair { global() struct
196 bytespair global() argument
[all...]
H A Dsockex3_kern.c23 #define PARSE_IPV6 4
51 __u64 w1 = load_word(ctx, off + 4); in ipv6_addr_hash()
78 struct pair { struct
86 __type(value, struct pair); argument
92 struct flow_key_record key = g->flow; in update_stats()
93 struct pair *value; in update_stats()
97 __sync_fetch_and_add(&value->packets, 1); in update_stats()
98 __sync_fetch_and_add(&value->bytes, skb->len); in update_stats()
100 struct pair val = {1, skb->len}; in update_stats()
109 __u32 nhoff = skb->cb[0]; in parse_ip_proto()
[all …]
/linux/fs/ntfs3/
H A Dlznt.c1 // SPDX-License-Identifier: GPL-2.0
4 * Copyright (C) 2019-2021 Paragon Software GmbH, All rights reserved.
17 // clang-format off
21 // clang-format on
55 ((40543U * ((((src[0] << 4) ^ src[1]) << 4) ^ src[2])) >> 4) & in longest_match_std()
56 (LZNT_CHUNK_SIZE - 1); in longest_match_std()
58 hash = &(ctx->hash[hash_index].p1); in longest_match_std()
60 if (hash[0] >= ctx->unc && hash[0] < src && hash[0][0] == src[0] && in longest_match_std()
63 if (ctx->max_len > 3) in longest_match_std()
64 len1 += get_match_len(src + 3, ctx->unc_end, in longest_match_std()
[all …]
/linux/Documentation/devicetree/bindings/sound/
H A Dfsl,qmc-audio.yaml1 # SPDX-License-Identifier: (GPL-2.0-only OR BSD-2-Clause)
3 ---
4 $id: http://devicetree.org/schemas/sound/fsl,qmc-audio.yaml#
5 $schema: http://devicetree.org/meta-schemas/core.yaml#
10 - Herve Codina <herve.codina@bootlin.com>
16 if only one QMC channel is used by the DAI or it is working in non-interleaved
20 - $ref: dai-common.yaml#
24 const: fsl,qmc-audio
26 '#address-cells':
28 '#size-cells':
[all …]
/linux/tools/testing/selftests/drivers/net/lib/py/
H A Denv.py1 # SPDX-License-Identifier: GPL-2.0
48 pair = line.split('=', maxsplit=1)
49 if len(pair) != 2:
51 env[pair[0]] = pair[1]
84 self.dev = ip("-d link show dev " + self.env['NETIF'], json=True)[0]
105 For local testing it creates two network namespaces and a pair
125 self.addr_v = { "4"
[all...]
/linux/lib/raid6/
H A Drecov_neon_inner.c1 // SPDX-License-Identifier: GPL-2.0-only
13 * implement the underlying instruction. AArch32 only provides a 64-bit
20 uint8x8x2_t pair; in vqtbl1q_u8() member
23 return vcombine_u8(vtbl2_u8(__a.pair, vget_low_u8(b)), in vqtbl1q_u8()
24 vtbl2_u8(__a.pair, vget_high_u8(b))); in vqtbl1q_u8()
39 * while ( bytes-- ) { in __raid6_2data_recov_neon()
56 vy = vshrq_n_u8(vx, 4); in __raid6_2data_recov_neon()
61 vy = vshrq_n_u8(px, 4); in __raid6_2data_recov_neon()
70 bytes -= 16; in __raid6_2data_recov_neon()
86 * while (bytes--) { in __raid6_datap_recov_neon()
[all …]
/linux/tools/perf/
H A Dbuiltin-diff.c1 // SPDX-License-Identifier: GPL-2.0
3 * builtin-diff.c
23 #include "util/time-utils.h"
27 #include "util/block-info.h"
33 #include <subcmd/parse-options.h>
118 [COMPUTE_DELTA_ABS] = "delta-abs",
186 int ret = -EINVAL; in setup_compute_opt_wdiff()
224 return -EINVAL; in setup_compute_opt()
233 int *cp = (int *) opt->value; in setup_compute()
246 unsigned len = option++ - str; in setup_compute()
[all …]
/linux/include/linux/mtd/
H A Dmtd.h1 /* SPDX-License-Identifier: GPL-2.0-or-later */
3 * Copyright © 1999-2010 David Woodhouse <dwmw2@infradead.org> et al.
15 #include <linux/nvmem-provider.h>
17 #include <mtd/mtd-abi.h>
21 #define MTD_FAIL_ADDR_UNKNOWN -1LL
50 * struct mtd_oob_ops - oob operation operands
61 * @datbuf: data buffer - if NULL only oob data are read/written
65 * one go. If you try to do that on such an MTD device, -EINVAL will be
67 * devices you should split the write request into several sub-requests when the
83 * struct mtd_oob_region - oob region definition
[all …]
/linux/drivers/scsi/isci/
H A Dscu_task_context.h7 * Copyright(c) 2008 - 2011 Intel Corporation. All rights reserved.
20 * Foundation, Inc., 51 Franklin St - Fifth Floor, Boston, MA 02110-1301 USA.
26 * Copyright(c) 2008 - 2011 Intel Corporation. All rights reserved.
68 * enum scu_ssp_task_type - This enumberation defines the various SSP task
84 * enum scu_sata_task_type - This enumeration defines the various SATA task
222 * MAKE_SCU_CONTEXT_COMMAND_TYPE() -
279 (MAKE_SCU_CONTEXT_COMMAND_REQUEST(SCU_CONTEXT_COMMAND_REQUEST_TYPE_OTHER_RNC, 4))
293 * struct ssp_task_context - This is the SCU hardware definition for an SSP
327 * struct stp_task_context - This is the SCU hardware definition for an STP
335 u32 pm_port:4;
[all …]
/linux/arch/arc/include/asm/
H A Ddsp-impl.h1 /* SPDX-License-Identifier: GPL-2.0-only */
28 /* clobbers r10, r11 registers pair */
33 * able to break kernel - reset it to DSP_CTRL_DISABLED_ALL value
50 /* clobbers r10, r11 registers pair */
70 * register with a core register) instead of LR + SR pair.
77 "ld %0, [%2, %4] \n" \
79 "st %0, [%1, %4] \n" \
100 long unsigned int *saveto = &prev->thread.dsp.ACC0_GLO; in dsp_save_restore()
101 long unsigned int *readfrom = &next->thread.dsp.ACC0_GLO; in dsp_save_restore()
/linux/drivers/net/ethernet/cisco/enic/
H A Dvnic_devcmd.h1 /* SPDX-License-Identifier: GPL-2.0-only */
3 * Copyright 2008-2010 Cisco Systems, Inc. All rights reserved.
15 #define _CMD_NMASK ((1 << _CMD_NBITS)-1)
16 #define _CMD_VTYPEMASK ((1 << _CMD_VTYPEBITS)-1)
17 #define _CMD_FLAGSMASK ((1 << _CMD_FLAGSBITS)-1)
18 #define _CMD_DIRMASK ((1 << _CMD_DIRBITS)-1)
45 #define _CMD_VTYPE_SCSI 4U
99 /* dev-specific block member:
109 CMD_STATS_DUMP = _CMDC(_CMD_DIR_WRITE, _CMD_VTYPE_ALL, 4),
176 * (u16)a1 & 0x0000ffff00000000=intr num (-1 for no intr)
[all …]
/linux/drivers/gpu/drm/i915/display/
H A Dintel_lvds_regs.h1 /* SPDX-License-Identifier: MIT */
18 /* Selects pipe B for LVDS data. Must be set on pre-965. */
29 /* Enable border for unscaled (or aspect-scaled) display */
32 * Enables the A0-A2 data pairs and CLKA, containing 18 bits of color data per
39 * Controls the A3 data pair, which contains the additional LSBs for 24 bit
47 * Controls the CLKB pair. This should only be set when LVDS_B0B3_POWER_UP
50 #define LVDS_CLKB_POWER_MASK REG_GENMASK(5, 4)
54 * Controls the B0-B3 data pairs. This must be set to match the DPLL p2
55 * setting for whether we are in dual-channel mode. The B3 pair will

12345678910>>...33