Received: by 2002:a05:6a10:8395:0:0:0:0 with SMTP id n21csp257658pxh; Tue, 9 Nov 2021 10:13:26 -0800 (PST) X-Google-Smtp-Source: ABdhPJyWxtVFbZWUiBV96390AEA4buOitWwCL8AjLWx8CPPTth085upqXvhOrU/Uxz7bZ7CHvGBY X-Received: by 2002:a17:907:7ba2:: with SMTP id ne34mr11789183ejc.290.1636481605922; Tue, 09 Nov 2021 10:13:25 -0800 (PST) ARC-Seal: i=1; a=rsa-sha256; t=1636481605; cv=none; d=google.com; s=arc-20160816; b=jw052deAyuyRYwB6JuBvpIutGKfnzcdwzXn3H7LFypj7m/g3rzFpCXKZQtKIrlZWaO heOug78hwVSQl18OdxEyR1yC0SddiEJ+hALNQXkIop5QdoLPQ6Y3tbThsD7ziPaZ9jPO rIDFi6jE0wscw0f7SGbUQsSrVY1ngqQEczwDiy2/L23oX1HnqyS8lmG4+vbhkMXx6AbU O1dy4oHHUH6dTwfifeWjCVf/0BYBt3I55WkiQYU0ueuJJwJNBFz/NJyjx2xw9NXYTBEx 3XTa1NTTJ1GlflKvUVmLUFnKTIkJO0vVL/d/eeTSn0/CvOlSP1etCPf6Us1htbKVztaG vOBg== ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=arc-20160816; h=list-id:precedence:content-transfer-encoding:mime-version :references:in-reply-to:message-id:date:subject:to:from :dkim-signature; bh=pSiPeFKJFYMukSt/z6kM3xPQTQJ5rRNs0AebXPpOAjY=; b=SyVdoAsYDvL1DmXnaJGM4+pxHRjyRqfgBPBsKKGRiyr6Sg+Wk8eVzxqZk44jeseNrd n/toCksh+eJCeqFLQifknYdijYJ5gYdhUrSE0dPZfES+N2bq/VYPTFSO3gwBzwrgwOdo SIgyi1py+y37Pb945bIk61DQtp1yNqa/O8LDFWrrfZB8rzw50JyYjWsaMVDx/P8kU55g 1blPTEFjCmUnU6hUqMR4L/43qZEITH170CONtPl2bj6eNV7/9sG58gpI5qD4Mzd8ilB2 F47wxpGnaIdxkRhxgCLrxWsQXCV0q86b5J3LRt516LCAU6poB2MxAPpnuH50Y73bjgPo FG5w== ARC-Authentication-Results: i=1; mx.google.com; dkim=pass header.i=@sifive.com header.s=google header.b=mSA9WxR9; spf=pass (google.com: domain of linux-kernel-owner@vger.kernel.org designates 23.128.96.18 as permitted sender) smtp.mailfrom=linux-kernel-owner@vger.kernel.org Return-Path: Received: from vger.kernel.org (vger.kernel.org. [23.128.96.18]) by mx.google.com with ESMTP id di3si38124687ejc.158.2021.11.09.10.12.58; Tue, 09 Nov 2021 10:13:25 -0800 (PST) Received-SPF: pass (google.com: domain of linux-kernel-owner@vger.kernel.org designates 23.128.96.18 as permitted sender) client-ip=23.128.96.18; Authentication-Results: mx.google.com; dkim=pass header.i=@sifive.com header.s=google header.b=mSA9WxR9; spf=pass (google.com: domain of linux-kernel-owner@vger.kernel.org designates 23.128.96.18 as permitted sender) smtp.mailfrom=linux-kernel-owner@vger.kernel.org Received: (majordomo@vger.kernel.org) by vger.kernel.org via listexpand id S245013AbhKIJwV (ORCPT + 99 others); Tue, 9 Nov 2021 04:52:21 -0500 Received: from lindbergh.monkeyblade.net ([23.128.96.19]:49246 "EHLO lindbergh.monkeyblade.net" rhost-flags-OK-OK-OK-OK) by vger.kernel.org with ESMTP id S244296AbhKIJvh (ORCPT ); Tue, 9 Nov 2021 04:51:37 -0500 Received: from mail-pl1-x632.google.com (mail-pl1-x632.google.com [IPv6:2607:f8b0:4864:20::632]) by lindbergh.monkeyblade.net (Postfix) with ESMTPS id 09443C061226 for ; Tue, 9 Nov 2021 01:48:48 -0800 (PST) Received: by mail-pl1-x632.google.com with SMTP id n8so19936158plf.4 for ; Tue, 09 Nov 2021 01:48:48 -0800 (PST) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=sifive.com; s=google; h=from:to:subject:date:message-id:in-reply-to:references:mime-version :content-transfer-encoding; bh=pSiPeFKJFYMukSt/z6kM3xPQTQJ5rRNs0AebXPpOAjY=; b=mSA9WxR92Ql2MISDabj0bHJAFDZkUwT81JIEMYpKz8W+M9Pvp4uemjF3gyefJwCwq8 Kx1kFXqDifT6/VW4sp7c1AepBIViPr1K2bGXhDuhia0TqwSJUAOUeu2ORw2HSSoYczyM 2HFCiI2ts6M0itgnhM7GS8YdbOsK3wx5zj1ICg6w4a9n9ruNhB5Qpe65mvi2WA6KlGiF xPT2A6QVPHSDVLKNKfhvNSzsCe5HpccBhPxYcQnyJvXT3PjwcC/JoAAUMBjVnj6DuRQ0 DSNNMBU7lBWr8kSELDsK30/YoTrw6FaxXRSdw/ZzXzMzNzi1DmBQfw+FXh/ZcdJLwdkq h4NA== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20210112; h=x-gm-message-state:from:to:subject:date:message-id:in-reply-to :references:mime-version:content-transfer-encoding; bh=pSiPeFKJFYMukSt/z6kM3xPQTQJ5rRNs0AebXPpOAjY=; b=h+DJDJiDxu5Ud1OMX5nXDXrXzcz5ClnOSfa0ncxU5mesoqKkbt7lyvVo8tHUXBXQ4q OUFIWiTl1TDRkTV9RMaBspIUmxkesrt+6L09RPM9wgNxj19o8lUm5exEa//YM98e0OR0 VaVlOZyu7Yk/+itYnXWsyxkhnaqbwNF82TCkrx5X90joHCN4W3aAGTApg+JPo5YF11+i AXj6SdYcOSu89o7rAgdWxbg/19C3nmgd31S0mX46eaI9LhuAPSGyGed4fU6vUkK2IP3s C0xgkAul7Pk4E4gIMJpB4Yym+iEJ5YbfYpz6SMN4t6stqZH9ZCHaOsL9Rv4gyzsK7+SE 071A== X-Gm-Message-State: AOAM530kcDAf3DKo8dB+KbUxnq6dwjGKdPL5EvtDpkuydxqZuBj5EQFA +oibqFzYk2RlBb6YF65lrh+ZXw== X-Received: by 2002:a17:902:c20d:b0:142:1009:585d with SMTP id 13-20020a170902c20d00b001421009585dmr5659968pll.83.1636451327530; Tue, 09 Nov 2021 01:48:47 -0800 (PST) Received: from hsinchu16.internal.sifive.com (59-124-168-89.hinet-ip.hinet.net. [59.124.168.89]) by smtp.gmail.com with ESMTPSA id cv1sm1940511pjb.48.2021.11.09.01.48.46 (version=TLS1_3 cipher=TLS_AES_256_GCM_SHA384 bits=256/256); Tue, 09 Nov 2021 01:48:47 -0800 (PST) From: Greentime Hu To: palmer@dabbelt.com, paul.walmsley@sifive.com, linux-riscv@lists.infradead.org, linux-kernel@vger.kernel.org, aou@eecs.berkeley.edu Subject: [PATCH v9 10/17] riscv: Add ptrace vector support Date: Tue, 9 Nov 2021 17:48:22 +0800 Message-Id: <2b593b387db3e7e3f9612fe76893b20d9b9e23a9.1636362169.git.greentime.hu@sifive.com> X-Mailer: git-send-email 2.31.1 In-Reply-To: References: MIME-Version: 1.0 Content-Transfer-Encoding: 8bit Precedence: bulk List-ID: X-Mailing-List: linux-kernel@vger.kernel.org This patch adds ptrace support for riscv vector. The vector registers will be saved in datap pointer of __riscv_v_state. This pointer will be set right after the __riscv_v_state data structure then it will be put in ubuf for ptrace system call to get or set. It will check if the datap got from ubuf is set to the correct address or not when the ptrace system call is trying to set the vector registers. Co-developed-by: Vincent Chen Signed-off-by: Vincent Chen Signed-off-by: Greentime Hu --- arch/riscv/include/uapi/asm/ptrace.h | 14 ++++++ arch/riscv/kernel/ptrace.c | 71 ++++++++++++++++++++++++++++ include/uapi/linux/elf.h | 1 + 3 files changed, 86 insertions(+) diff --git a/arch/riscv/include/uapi/asm/ptrace.h b/arch/riscv/include/uapi/asm/ptrace.h index bd3b8a710246..c3760395236c 100644 --- a/arch/riscv/include/uapi/asm/ptrace.h +++ b/arch/riscv/include/uapi/asm/ptrace.h @@ -83,11 +83,25 @@ struct __riscv_v_state { unsigned long vtype; unsigned long vcsr; void *datap; + /* + * In signal handler, datap will be set a correct user stack offset + * and vector registers will be copied to the address of datap + * pointer. + * + * In ptrace syscall, datap will be set to zero and the vector + * registers will be copied to the address right after this + * structure. + */ #if __riscv_xlen == 32 __u32 __padding; #endif }; +/* + * To define a practical maximum vlenb for ptrace and it may need to be + * extended someday. + */ +#define RISCV_MAX_VLENB (16384) #endif /* __ASSEMBLY__ */ #endif /* _UAPI_ASM_RISCV_PTRACE_H */ diff --git a/arch/riscv/kernel/ptrace.c b/arch/riscv/kernel/ptrace.c index 9c0511119bad..0bc11a70090c 100644 --- a/arch/riscv/kernel/ptrace.c +++ b/arch/riscv/kernel/ptrace.c @@ -27,6 +27,9 @@ enum riscv_regset { #ifdef CONFIG_FPU REGSET_F, #endif +#ifdef CONFIG_VECTOR + REGSET_V, +#endif }; static int riscv_gpr_get(struct task_struct *target, @@ -85,6 +88,64 @@ static int riscv_fpr_set(struct task_struct *target, } #endif +#ifdef CONFIG_VECTOR +static int riscv_vr_get(struct task_struct *target, + const struct user_regset *regset, + struct membuf to) +{ + struct __riscv_v_state *vstate = &target->thread.vstate; + + /* + * Ensure the vector registers have been saved to the memory before + * copying them to membuf. + */ + if (target == current) + vstate_save(current, task_pt_regs(current)); + + /* Copy vector header from vstate. */ + membuf_write(&to, vstate, RISCV_V_STATE_DATAP); + membuf_zero(&to, sizeof(void *)); +#if __riscv_xlen == 32 + membuf_zero(&to, sizeof(__u32)); +#endif + + /* Copy all the vector registers from vstate. */ + return membuf_write(&to, vstate->datap, riscv_vsize); +} + +static int riscv_vr_set(struct task_struct *target, + const struct user_regset *regset, + unsigned int pos, unsigned int count, + const void *kbuf, const void __user *ubuf) +{ + int ret, size; + struct __riscv_v_state *vstate = &target->thread.vstate; + + /* Copy rest of the vstate except datap and __padding. */ + ret = user_regset_copyin(&pos, &count, &kbuf, &ubuf, vstate, 0, + RISCV_V_STATE_DATAP); + if (unlikely(ret)) + return ret; + + /* Skip copy datap. */ + size = sizeof(vstate->datap); + count -= size; + ubuf += size; +#if __riscv_xlen == 32 + /* Skip copy _padding. */ + size = sizeof(vstate->__padding); + count -= size; + ubuf += size; +#endif + + /* Copy all the vector registers. */ + pos = 0; + ret = user_regset_copyin(&pos, &count, &kbuf, &ubuf, vstate->datap, + 0, riscv_vsize); + return ret; +} +#endif + static const struct user_regset riscv_user_regset[] = { [REGSET_X] = { .core_note_type = NT_PRSTATUS, @@ -104,6 +165,16 @@ static const struct user_regset riscv_user_regset[] = { .set = riscv_fpr_set, }, #endif +#ifdef CONFIG_VECTOR + [REGSET_V] = { + .core_note_type = NT_RISCV_VECTOR, + .align = 16, + .n = (32 * RISCV_MAX_VLENB)/sizeof(__u32), + .size = sizeof(__u32), + .regset_get = riscv_vr_get, + .set = riscv_vr_set, + }, +#endif }; static const struct user_regset_view riscv_user_native_view = { diff --git a/include/uapi/linux/elf.h b/include/uapi/linux/elf.h index 61bf4774b8f2..60c5b873a8f6 100644 --- a/include/uapi/linux/elf.h +++ b/include/uapi/linux/elf.h @@ -432,6 +432,7 @@ typedef struct elf64_shdr { #define NT_MIPS_DSP 0x800 /* MIPS DSP ASE registers */ #define NT_MIPS_FP_MODE 0x801 /* MIPS floating-point mode */ #define NT_MIPS_MSA 0x802 /* MIPS SIMD registers */ +#define NT_RISCV_VECTOR 0x900 /* RISC-V vector registers */ /* Note types with note name "GNU" */ #define NT_GNU_PROPERTY_TYPE_0 5 -- 2.31.1