From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: X-Spam-Checker-Version: SpamAssassin 3.4.0 (2014-02-07) on aws-us-west-2-korg-lkml-1.web.codeaurora.org Received: from kanga.kvack.org (kanga.kvack.org [205.233.56.17]) by smtp.lore.kernel.org (Postfix) with ESMTP id 7104AC47DDF for ; Thu, 25 Jan 2024 06:30:25 +0000 (UTC) Received: by kanga.kvack.org (Postfix) id 158508D000D; Thu, 25 Jan 2024 01:30:21 -0500 (EST) Received: by kanga.kvack.org (Postfix, from userid 40) id 0BA4C8D000C; Thu, 25 Jan 2024 01:30:21 -0500 (EST) X-Delivered-To: int-list-linux-mm@kvack.org Received: by kanga.kvack.org (Postfix, from userid 63042) id DD8D08D000D; Thu, 25 Jan 2024 01:30:20 -0500 (EST) X-Delivered-To: linux-mm@kvack.org Received: from relay.hostedemail.com (smtprelay0015.hostedemail.com [216.40.44.15]) by kanga.kvack.org (Postfix) with ESMTP id C65858D000C for ; Thu, 25 Jan 2024 01:30:20 -0500 (EST) Received: from smtpin01.hostedemail.com (a10.router.float.18 [10.200.18.1]) by unirelay10.hostedemail.com (Postfix) with ESMTP id 8BAD1C07B3 for ; Thu, 25 Jan 2024 06:30:20 +0000 (UTC) X-FDA: 81716859000.01.B2DD7B5 Received: from mail-oo1-f43.google.com (mail-oo1-f43.google.com [209.85.161.43]) by imf29.hostedemail.com (Postfix) with ESMTP id CBC5A120028 for ; Thu, 25 Jan 2024 06:30:18 +0000 (UTC) Authentication-Results: imf29.hostedemail.com; dkim=pass header.d=rivosinc-com.20230601.gappssmtp.com header.s=20230601 header.b=rERrXiap; spf=pass (imf29.hostedemail.com: domain of debug@rivosinc.com designates 209.85.161.43 as permitted sender) smtp.mailfrom=debug@rivosinc.com; dmarc=none ARC-Message-Signature: i=1; a=rsa-sha256; c=relaxed/relaxed; d=hostedemail.com; s=arc-20220608; t=1706164218; h=from:from:sender:reply-to:subject:subject:date:date: message-id:message-id:to:to:cc:cc:mime-version:mime-version: content-type:content-transfer-encoding:content-transfer-encoding: in-reply-to:in-reply-to:references:references:dkim-signature; bh=4ROIIq+tfSuVQ8U/gtdFWUWXai61z50x8X9vsARg+kI=; b=49v+5U3D5g/MmvzxLVtLL91aF0iH9IQI3pw1rgI1QcnMfns0jR11CSfapmA3R0iYpR2Zag EHh4/l4N47lQ0amLh5o4fn85B5KVF7f36qNXBeL6cj/MZoHBdsYrMItoQ/kXBIrGrry2Uc lktIngkfzOLJb0q0oRY4jvqmHbVIBqw= ARC-Seal: i=1; s=arc-20220608; d=hostedemail.com; t=1706164218; a=rsa-sha256; cv=none; b=w8dPE4D84VeXekRnpyqUkaYyVRSzkddXs8kNR2Og+Wq0hDgAW7Tr9qyGWRYOfaLbztmBcM c/vxaGWqls536OAnaGrsA1i2wT9oH7qkfBkHU2WIS/nYBGWIoFgkRoLhv9h4wX3surYy/X qWE20eUDcpJMnpcOTSJFy7pgiVY1hhI= ARC-Authentication-Results: i=1; imf29.hostedemail.com; dkim=pass header.d=rivosinc-com.20230601.gappssmtp.com header.s=20230601 header.b=rERrXiap; spf=pass (imf29.hostedemail.com: domain of debug@rivosinc.com designates 209.85.161.43 as permitted sender) smtp.mailfrom=debug@rivosinc.com; dmarc=none Received: by mail-oo1-f43.google.com with SMTP id 006d021491bc7-595aa5b1fe0so3979209eaf.2 for ; Wed, 24 Jan 2024 22:30:18 -0800 (PST) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=rivosinc-com.20230601.gappssmtp.com; s=20230601; t=1706164218; x=1706769018; darn=kvack.org; h=content-transfer-encoding:mime-version:references:in-reply-to :message-id:date:subject:cc:to:from:from:to:cc:subject:date :message-id:reply-to; bh=4ROIIq+tfSuVQ8U/gtdFWUWXai61z50x8X9vsARg+kI=; b=rERrXiaptQCllKPlxmgS0ZqfsOwpFj0aO2C4KQNgbA/FDNlu8w95mjr2I1EwITopSO pJGFHJymrhZXfN6sQ53AyEQwWwyQ8UjPFtMiMBeSp1BrMr4J3FHDfoVgtL+QcS6e6yY7 i/JvkqdEy5LNjzkQhkU4+CoRoUA47JS6xjVOu5aWfC8KoNKzha5cuJjRf3R4I7izdQFH QX0K0zyoUuC2w/XZNm5gl0KAj9615V6NWPIQpOs05y07xT7TaU7+gbExa7uevJSDIgTL gBSGvWPlT1Zt+8w4D67LF5vsAa7R5XKRKSeeeszOWZo4GFKhL+SCE0xwgfQjTKSSg63W xZnA== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20230601; t=1706164218; x=1706769018; h=content-transfer-encoding:mime-version:references:in-reply-to :message-id:date:subject:cc:to:from:x-gm-message-state:from:to:cc :subject:date:message-id:reply-to; bh=4ROIIq+tfSuVQ8U/gtdFWUWXai61z50x8X9vsARg+kI=; b=kCGUo54AkQrsWoZ8ClJjxVn8FvJcb97ve+TomKODdFFgGVGDaVgfGR2TbhdV1GEAP4 7jpT/L+9oDkOPgxmxneYo+AGJI0fWibsc5k3KZrBN7bl4lQOxXqOLN9MGSB4tL76icw4 qBj52+mqSrsVwE2qx+l6zZTE+RmJoaMCf2+i4Jmtw7msufzCRRA6e+7DLB4vqPoqcIsk uCeyOSj0ZsObNLO3PEG+ra9v5QcSXY2a/rdRGZuqjkgC7n/ffkOWKNdcPfkavgP+4aVS GQEMXBTE0OdZ+AZ3/sCsjZSSRp36bOi+p3c0WY80CL85Epw8HNnnLNO0v+dq7UvfX7h6 vjGw== X-Gm-Message-State: AOJu0YxO7VeyZnKfm4Wpi5+8jZt52zTnbLdDdwAtpPLGqJ4TjE9Y2CCv XuwCeSMUBOku/ImyGy5nWbcCiZGvqcCaN5dfocgarqchdJLgClXLgr0EuB/nMKc= X-Google-Smtp-Source: AGHT+IFCTO1aRpreluHW/C5C9tNmtfREjRA/JGLkNEyuOfgIi16e6JM3wL9ZmcIo8frDDBAlk8/Blw== X-Received: by 2002:a05:6358:94a9:b0:176:1227:8735 with SMTP id i41-20020a05635894a900b0017612278735mr688376rwb.58.1706164217947; Wed, 24 Jan 2024 22:30:17 -0800 (PST) Received: from debug.ba.rivosinc.com ([64.71.180.162]) by smtp.gmail.com with ESMTPSA id t19-20020a056a00139300b006dd870b51b8sm3201139pfg.126.2024.01.24.22.30.14 (version=TLS1_3 cipher=TLS_AES_256_GCM_SHA384 bits=256/256); Wed, 24 Jan 2024 22:30:17 -0800 (PST) From: debug@rivosinc.com To: rick.p.edgecombe@intel.com, broonie@kernel.org, Szabolcs.Nagy@arm.com, kito.cheng@sifive.com, keescook@chromium.org, ajones@ventanamicro.com, paul.walmsley@sifive.com, palmer@dabbelt.com, conor.dooley@microchip.com, cleger@rivosinc.com, atishp@atishpatra.org, alex@ghiti.fr, bjorn@rivosinc.com, alexghiti@rivosinc.com Cc: corbet@lwn.net, aou@eecs.berkeley.edu, oleg@redhat.com, akpm@linux-foundation.org, arnd@arndb.de, ebiederm@xmission.com, shuah@kernel.org, brauner@kernel.org, debug@rivosinc.com, guoren@kernel.org, samitolvanen@google.com, evan@rivosinc.com, xiao.w.wang@intel.com, apatel@ventanamicro.com, mchitale@ventanamicro.com, waylingii@gmail.com, greentime.hu@sifive.com, heiko@sntech.de, jszhang@kernel.org, shikemeng@huaweicloud.com, david@redhat.com, charlie@rivosinc.com, panqinglin2020@iscas.ac.cn, willy@infradead.org, vincent.chen@sifive.com, andy.chiu@sifive.com, gerg@kernel.org, jeeheng.sia@starfivetech.com, mason.huo@starfivetech.com, ancientmodern4@gmail.com, mathis.salmen@matsal.de, cuiyunhui@bytedance.com, bhe@redhat.com, chenjiahao16@huawei.com, ruscur@russell.cc, bgray@linux.ibm.com, alx@kernel.org, baruch@tkos.co.il, zhangqing@loongson.cn, catalin.marinas@arm.com, revest@chromium.org, josh@joshtriplett.org, joey.gouly@arm.com, shr@devkernel.io, omosnace@redhat.com, ojeda@kernel.org, jhubbard@nvidia.com, linux-doc@vger.kernel.org, linux-riscv@lists.infradead.org, linux-kernel@vger.kernel.org, linux-mm@kvack.org, linux-arch@vger.kernel.org, linux-kselftest@vger.kernel.org Subject: [RFC PATCH v1 22/28] riscv sigcontext: adding cfi state field in sigcontext Date: Wed, 24 Jan 2024 22:21:47 -0800 Message-ID: <20240125062739.1339782-23-debug@rivosinc.com> X-Mailer: git-send-email 2.43.0 In-Reply-To: <20240125062739.1339782-1-debug@rivosinc.com> References: <20240125062739.1339782-1-debug@rivosinc.com> MIME-Version: 1.0 Content-Transfer-Encoding: 8bit X-Stat-Signature: pjicmcrdicsebfedbtr93bysbbjhb9ki X-Rspamd-Server: rspam10 X-Rspamd-Queue-Id: CBC5A120028 X-Rspam-User: X-HE-Tag: 1706164218-899599 X-HE-Meta: U2FsdGVkX18Cdi4Fs3t7m/OwaRuX/GDS8Epr0t0fa1xWHnYyA09PLurU21D02KA2Vkd3yawW7l6z/ax64zuVvjO4ECt3lLoq0wCBxwCtnxNPkahFGE+p/if3HMoX4D/AZXc6XpS/Cg7NKUSAdkZbA6nhe+3k6PfabtpuBB6rPED7C1hN2kNyPRPowmQvgineShi1KPobdc3Ktx9/dPES0KJzBkdYfQreFsfc4sc1BC/AxeEuxrH+OixddvITzwm0avp/Xdzb3nm5RnhfOO2s42MJKxVWDAdV0yVTjnXcyxcNdwYM2Gq/VjrruC3pFOt0kq1Y4F9K0khl3Je+UCdlm2evNfPbB3IUsxQsOmrIsCadqGF98ZM4VT5j66hmS/tY7VlSt9fKNPTBXdD16Lx0wt5ikSzrAoi81hdPtTxJRnYWqRytr3FcUWZwLwzt/k0ByAJ9CBlAr/9gNhCZzzo+L54c4AbmWe7WLgFvXzFxJaX2p9FYU2AAhs0GUVwbn+cfRzWr15MMetook5KOVzIjhB735Pf2vC7ozONLYkalI/IoZCJufQmOYYSMDnhwir92odLmQxZeb2QUK1kXy2h+Znu9r8aa8Nf9jqmuASZAyFgrDtRqcG/kSdceUUKY+JNnNuJOqyv6LiR7lNbstKItrq1YDe42DS24/WyuKiVDKXZ3K23diBaIpWnSzu6k3irzKiQk0RNBrLwzX2sDhphRMyBpJoNUzBasNPBHL6hVO7od7hzxGI7PMAz5kvsTkBi+1zCwllyNUcojje8ymf9RONp8irgjqWj1xFoIXYBf7Wy2sD1hAzrUnpHlcJSggv3fEhKlHuhIzgy6qZrmn2dHvlN4UcRMFG0eTIGyiOHpqDfCAHzSJcKRhUClbm5JrrKc/ArXO2D2E/4AFKSc1YOLYylARJdi+fAie41ajjJ8EjMnwU7KvOfGcYiC9iNO8OJ2iTRcPF60ChqXABJxtaP p5kwzwYz LS1duOQm5AOyLkw73Y+MKvf8L3qzgaWQrMyYOgwtrgPIVLFbQG3MrAQd8KIX2ZDX7AH/S0dynxMYiTGn2P2fuMHvAaBi9f22n4D7ZH7ITsr9Nvz9URc5By0gdgIj4hrROIYZb/4dzKiI7xVxBjz1b3XE81C6fiUIh+bRLclpS77t/x/tDBBZR0e+WDwmd8J3d9BE4dWcviWkB0RHhWP3mG5qKJIrhIoS4FCIptLlTU9DMtgmkDTC6EeYPGUoOwK/IIY3spnwE7zs9y9N9sSpKWuo6gna1+88XKln8b7Ag3WxwLjF2CuhhvMPWeeTsYkTpm588d6iisL4plT+3Fn1sORMxjC1G3B+OHyuI8PrmIK60UcN7gwwV5ImshV0rA0kkb7xugACleM6GDm18AWx+5M4pyY9WRUH/WCEHyljatH+xCeilqDqVyEX5aPmLKYC9Lu4a X-Bogosity: Ham, tests=bogofilter, spamicity=0.000001, version=1.2.4 Sender: owner-linux-mm@kvack.org Precedence: bulk X-Loop: owner-majordomo@kvack.org List-ID: List-Subscribe: List-Unsubscribe: From: Deepak Gupta Shadow stack needs to be saved and restored on signal delivery and signal return. sigcontext embedded in ucontext is extendible. Adding cfi state in there which can be used to save cfi state before signal delivery and restore cfi state on sigreturn Signed-off-by: Deepak Gupta --- arch/riscv/include/uapi/asm/sigcontext.h | 5 +++++ 1 file changed, 5 insertions(+) diff --git a/arch/riscv/include/uapi/asm/sigcontext.h b/arch/riscv/include/uapi/asm/sigcontext.h index cd4f175dc837..5ccdd94a0855 100644 --- a/arch/riscv/include/uapi/asm/sigcontext.h +++ b/arch/riscv/include/uapi/asm/sigcontext.h @@ -21,6 +21,10 @@ struct __sc_riscv_v_state { struct __riscv_v_ext_state v_state; } __attribute__((aligned(16))); +struct __sc_riscv_cfi_state { + unsigned long ss_ptr; /* shadow stack pointer */ + unsigned long rsvd; /* keeping another word reserved in case we need it */ +}; /* * Signal context structure * @@ -29,6 +33,7 @@ struct __sc_riscv_v_state { */ struct sigcontext { struct user_regs_struct sc_regs; + struct __sc_riscv_cfi_state sc_cfi_state; union { union __riscv_fp_state sc_fpregs; struct __riscv_extra_ext_header sc_extdesc; -- 2.43.0