Home
last modified time | relevance | path

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

12345678910>>...39

/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 …]
H A Dfsl_easrc.c1 // SPDX-License-Identifier: GPL-2.0
7 #include <linux/dma-mapping.h>
32 #include "imx-pcm.h"
51 struct fsl_easrc_priv *easrc_priv = easrc->private; in fsl_easrc_iec958_put_bits()
53 (struct soc_mreg_control *)kcontrol->private_value; in fsl_easrc_iec958_put_bits()
54 unsigned int regval = ucontrol->value.integer.value[0]; in fsl_easrc_iec958_put_bits()
56 easrc_priv->bps_iec958[mc->regbase] = regval; in fsl_easrc_iec958_put_bits()
66 struct fsl_easrc_priv *easrc_priv = easrc->private; in fsl_easrc_iec958_get_bits()
68 (struct soc_mreg_control *)kcontrol->private_value; in fsl_easrc_iec958_get_bits()
70 ucontrol->value.enumerated.item[0] = easrc_priv->bps_iec958[mc->regbase]; in fsl_easrc_iec958_get_bits()
[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/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 …]
/linux/Documentation/ABI/testing/
H A Dsysfs-driver-qat_rl4 Contact: qat-linux@intel.com
39 Contact: qat-linux@intel.com
45 The value is a 64-bit bit mask and is written/displayed in hex.
46 Each bit of this mask represents a single ring pair i.e.,
47 bit 1 == ring pair id 0; bit 3 == ring pair id 2.
51 assigned to a certain ring pair can be checked by querying
54 The maximum number of ring pairs is 4 per SLA.
64 # echo 4 > /sys/bus/pci/devices/<BDF>/qat_rl/id
76 Contact: qat-linux@intel.com
96 4
[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/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/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()
[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/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/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/tools/perf/tests/
H A Dcpumap.c1 // SPDX-License-Identifier: GPL-2.0
6 #include "util/synthetic-events.h"
19 struct perf_record_cpu_map *map_event = &event->cpu_map; in process_event_mask()
24 data = &map_event->data; in process_event_mask()
26 TEST_ASSERT_VAL("wrong type", data->type == PERF_CPU_MAP__MASK); in process_event_mask()
28 long_size = data->mask32_data.long_size; in process_event_mask()
30 TEST_ASSERT_VAL("wrong long_size", long_size == 4 || long_size == 8); in process_event_mask()
32 TEST_ASSERT_VAL("wrong nr", data->mask32_data.nr == 1); in process_event_mask()
44 TEST_ASSERT_VAL("wrong cpu", perf_cpu_map__cpu(map, i - 1).cpu == i); in process_event_mask()
55 struct perf_record_cpu_map *map_event = &event->cpu_map; in process_event_cpus()
[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/testing/selftests/drivers/net/lib/py/
H A Denv.py1 # SPDX-License-Identifier: GPL-2.0
45 pair = line.split('=', maxsplit=1)
46 if len(pair) != 2:
48 env[pair[0]] = pair[1]
65 self.dev = ip("-d link show dev " + self.env['NETIF'], json=True)[0]
97 For local testing it creates two network namespaces and a pair
117 self.addr_v = { "4": None, "6": None }
118 self.remote_addr_v = { "4": None, "6": None }
125 self.dev = ip("-d link show dev " + self.env['NETIF'], json=True)[0]
127 self.addr_v["4"] = self.env.get("LOCAL_V4")
[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/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/crypto/intel/qat/qat_6xxx/
H A Dadf_6xxx_hw_data.c1 // SPDX-License-Identifier: GPL-2.0-only
33 #define ADF_AE_GROUP_1 GENMASK(7, 4)
138 return -EINVAL; in get_service()
189 return -EINVAL; in get_rp_config()
215 /* If ASYM is enabled, use additional ring pair */ in get_rp_config()
221 return -EINVAL; in get_rp_config()
245 * Each group of 4 bits in the mask corresponds to a thread, with each bit in adf_gen6_get_arb_mask()
246 * indicating whether a job from a ring pair can be scheduled on that thread. in adf_gen6_get_arb_mask()
247 * The use of 4 bits is due to the organization of ring pairs into groups of in adf_gen6_get_arb_mask()
255 thd2arb_mask |= ring_mask << (thrd * 4); in adf_gen6_get_arb_mask()
[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/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>>...39