Message ID | 20240327200157.1097089-6-samuel.holland@sifive.com (mailing list archive) |
---|---|
State | New, archived |
Headers | show
Return-Path: <linux-arm-kernel-bounces+linux-arm-kernel=archiver.kernel.org@lists.infradead.org> X-Spam-Checker-Version: SpamAssassin 3.4.0 (2014-02-07) on aws-us-west-2-korg-lkml-1.web.codeaurora.org Received: from bombadil.infradead.org (bombadil.infradead.org [198.137.202.133]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.lore.kernel.org (Postfix) with ESMTPS id 9F28CCD1287 for <linux-arm-kernel@archiver.kernel.org>; Wed, 27 Mar 2024 21:18:40 +0000 (UTC) DKIM-Signature: v=1; a=rsa-sha256; q=dns/txt; c=relaxed/relaxed; d=lists.infradead.org; s=bombadil.20210309; h=Sender: Content-Transfer-Encoding:Content-Type:List-Subscribe:List-Help:List-Post: List-Archive:List-Unsubscribe:List-Id:MIME-Version:References:In-Reply-To: Message-ID:Date:Subject:Cc:To:From:Reply-To:Content-ID:Content-Description: Resent-Date:Resent-From:Resent-Sender:Resent-To:Resent-Cc:Resent-Message-ID: List-Owner; bh=Ldi8L8i9UovCU1OLLis0jcW77Hu6j0xAYwDk+au3g9I=; b=rllZQiLt4c5HAc 4x8d+d4mbTCRasPn7DA2BNO9ojAr0dtXtI2uRNMIaeQdyOeA4ji8+X+5oBnRBmo7YaQfnrP62sNnU T3Hqdu2U1zAyazyCp11/9/pVgkL5zCeK2mfiJdm7UYr/5u2rIPW1TOIMLGGsCsIcSCKrSsWRhAcU3 4NFkgbNqwmT21pFDdkgYjvcUXR4qcfz2HWnQiYEYYE6pttlhWHS0HpMGC0ZmopsdGh5xZM2PDcaru n5gLstx/vIOxRT1rFse5AoMQHBmlBcw5JK5oakhsNr0nH801EDk+pUAvrF3lYWnh9qsuVVDy75s6M 5rvZas9ZM8XVx34vHY1A==; Received: from localhost ([::1] helo=bombadil.infradead.org) by bombadil.infradead.org with esmtp (Exim 4.97.1 #2 (Red Hat Linux)) id 1rpafF-0000000BBDt-224U; Wed, 27 Mar 2024 21:18:29 +0000 Received: from desiato.infradead.org ([2001:8b0:10b:1:d65d:64ff:fe57:4e05]) by bombadil.infradead.org with esmtps (Exim 4.97.1 #2 (Red Hat Linux)) id 1rpZTV-0000000Au8B-3WAl for linux-arm-kernel@bombadil.infradead.org; Wed, 27 Mar 2024 20:02:17 +0000 DKIM-Signature: v=1; a=rsa-sha256; q=dns/txt; c=relaxed/relaxed; d=infradead.org; s=desiato.20200630; h=Content-Transfer-Encoding:MIME-Version :References:In-Reply-To:Message-ID:Date:Subject:Cc:To:From:Sender:Reply-To: Content-Type:Content-ID:Content-Description; bh=s9egB7QSoDAHRW6tgRYqVd+NUTiSQfL/JcKX7OjtD5w=; b=KnCIwVmJNh4MzLjXUKDjLgp/FV ixJQkTbUH386bYXx2n8j4UUkIA9krt3mpEo4/9iAJWtw250nlTco8DQBJ/RkG4vstknP4PlnYMEHO kRzFVsKBxL1BFLKypmrd0wT77K8oNfVwnvqAdBUXuoOe+/umL7i2/JhQGbJQ9jB+xIdhcd8mio88p CykhWwgaZr8F0FOhIfTQQ2SFzayJEYWKjGfbUkbSbtclaSERBrLk24eEOasPbuJJOBbCQ0MytxWxw sEuPxTzPGtl+O/V4yPErKAVrlW1h/1ujXG4Or6t8/2ZcBsZzpwJrjVSlfwn0auPBK4I6SNzLbJx2B dAIEGXhQ==; Received: from mail-pl1-x62f.google.com ([2607:f8b0:4864:20::62f]) by desiato.infradead.org with esmtps (Exim 4.97.1 #2 (Red Hat Linux)) id 1rpZTL-00000000WpO-2wb9 for linux-arm-kernel@lists.infradead.org; Wed, 27 Mar 2024 20:02:16 +0000 Received: by mail-pl1-x62f.google.com with SMTP id d9443c01a7336-1e00d1e13a2so1945735ad.0 for <linux-arm-kernel@lists.infradead.org>; Wed, 27 Mar 2024 13:02:07 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=sifive.com; s=google; t=1711569726; x=1712174526; darn=lists.infradead.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=s9egB7QSoDAHRW6tgRYqVd+NUTiSQfL/JcKX7OjtD5w=; b=LfzU3ozRbFRP4ITlpFuPz2PDvUynGm+eXPd+Ue7DJiQGrLnyyR7i7Gyv1wrO37+/hI 3xyxbD88NNz+IJFeyrTtwyGXew+R9em3rvVM4TP7s+4c4yitns1P5VjPd1QmTNrPAC40 HjkYarEOnxh95qyjBQig7FdpIIgNKBg9C4q5xZ7pJ5inGNM+mUsu4Jx9EwttkEc+ekca VVySnIGYrKnyX969p3OfsKUE+hWo1CzMbaUElOMDKLyHEa1HVx+fXvVJSmygS7ErrfQS OaQKpsZH3GLzjz99HdQswXMTx2Pb0mEJ8+qFg0+0usebcF7B4uU/rzbA59mJzn16cyHX sk8Q== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20230601; t=1711569726; x=1712174526; 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=s9egB7QSoDAHRW6tgRYqVd+NUTiSQfL/JcKX7OjtD5w=; b=MJoLvfF1saYyVkWyGklvRp0sdg/Ky4H+sIhnIHP+VsYSMpNgoz9NC2tJQp2eqEOPYP c1lysuOgO6G/xJuENH0kty1iXUU4ycYN5z+w9yRb+39R4bdZDiTrlbEcGcCGsNhdFZLw xH7DwP9cF7C39tVLpGgSD7KoKk7xQhZjg4ueqmHJCGGNBbJ2+xaTqS8wEtxkNt4F8sgv NKxCmLhRf2dff2uHwTAqIgqOQNvv9KUYXuzMDbSFDKMXmB+2kLa6SfBCiqr8zWNkU0Xa Wrdz9No0tTZu2f+Op9V3B4daT/0Fs5dI4RLN6FaTW1Yuy7Zkx9p8nRkNu1uM3kyRsiRH x5PQ== X-Forwarded-Encrypted: i=1; AJvYcCUitWRZJ3v9Adm259bf25lu40eostllGSxPCmdwp3O6gCyOrnRBTcIBBAG45uemKlHBjO66nt9JWvs8RUHAN/ZochyyqJM6usunvyYVeocbiHzECcI= X-Gm-Message-State: AOJu0YyIT0+f0ZbyEvlc/AZAlPS/Smd0/n2agae57TIFhc2ujHwTaMB1 8S4qOX7sSajTZ3WSYWvku9OhzfFNwMu/A4vlak2S/MC/TPMEAyoT0aJ4acxGNYY= X-Google-Smtp-Source: AGHT+IFGHdi74bAZSMUCS5nBpcP7LI5Cfqz6VZFaIDx36rlYRojmLVaB4TIyZga5IdN5tuwaxR1nKA== X-Received: by 2002:a17:903:2b05:b0:1dc:a605:5435 with SMTP id mc5-20020a1709032b0500b001dca6055435mr854470plb.31.1711569725718; Wed, 27 Mar 2024 13:02:05 -0700 (PDT) Received: from sw06.internal.sifive.com ([4.53.31.132]) by smtp.gmail.com with ESMTPSA id u4-20020a170902e5c400b001dd0d0d26a4sm9446459plf.147.2024.03.27.13.02.04 (version=TLS1_3 cipher=TLS_AES_256_GCM_SHA384 bits=256/256); Wed, 27 Mar 2024 13:02:05 -0700 (PDT) From: Samuel Holland <samuel.holland@sifive.com> To: Andrew Morton <akpm@linux-foundation.org>, linux-arm-kernel@lists.infradead.org, x86@kernel.org Cc: linux-kernel@vger.kernel.org, linux-arch@vger.kernel.org, linuxppc-dev@lists.ozlabs.org, linux-riscv@lists.infradead.org, Christoph Hellwig <hch@lst.de>, loongarch@lists.linux.dev, amd-gfx@lists.freedesktop.org, Samuel Holland <samuel.holland@sifive.com>, Catalin Marinas <catalin.marinas@arm.com>, Will Deacon <will@kernel.org> Subject: [PATCH v3 05/14] arm64: crypto: Use CC_FLAGS_FPU for NEON CFLAGS Date: Wed, 27 Mar 2024 13:00:36 -0700 Message-ID: <20240327200157.1097089-6-samuel.holland@sifive.com> X-Mailer: git-send-email 2.43.1 In-Reply-To: <20240327200157.1097089-1-samuel.holland@sifive.com> References: <20240327200157.1097089-1-samuel.holland@sifive.com> MIME-Version: 1.0 X-CRM114-Version: 20100106-BlameMichelson ( TRE 0.8.0 (BSD) ) MR-646709E3 X-CRM114-CacheID: sfid-20240327_200207_950508_6BC8DDA7 X-CRM114-Status: GOOD ( 12.00 ) X-BeenThere: linux-arm-kernel@lists.infradead.org X-Mailman-Version: 2.1.34 Precedence: list List-Id: <linux-arm-kernel.lists.infradead.org> List-Unsubscribe: <http://lists.infradead.org/mailman/options/linux-arm-kernel>, <mailto:linux-arm-kernel-request@lists.infradead.org?subject=unsubscribe> List-Archive: <http://lists.infradead.org/pipermail/linux-arm-kernel/> List-Post: <mailto:linux-arm-kernel@lists.infradead.org> List-Help: <mailto:linux-arm-kernel-request@lists.infradead.org?subject=help> List-Subscribe: <http://lists.infradead.org/mailman/listinfo/linux-arm-kernel>, <mailto:linux-arm-kernel-request@lists.infradead.org?subject=subscribe> Content-Type: text/plain; charset="us-ascii" Content-Transfer-Encoding: 7bit Sender: "linux-arm-kernel" <linux-arm-kernel-bounces@lists.infradead.org> Errors-To: linux-arm-kernel-bounces+linux-arm-kernel=archiver.kernel.org@lists.infradead.org |
Series |
Unified cross-architecture kernel-mode FPU API
|
expand
|
diff --git a/arch/arm64/lib/Makefile b/arch/arm64/lib/Makefile index 29490be2546b..13e6a2829116 100644 --- a/arch/arm64/lib/Makefile +++ b/arch/arm64/lib/Makefile @@ -7,10 +7,8 @@ lib-y := clear_user.o delay.o copy_from_user.o \ ifeq ($(CONFIG_KERNEL_MODE_NEON), y) obj-$(CONFIG_XOR_BLOCKS) += xor-neon.o -CFLAGS_REMOVE_xor-neon.o += -mgeneral-regs-only -CFLAGS_xor-neon.o += -ffreestanding -# Enable <arm_neon.h> -CFLAGS_xor-neon.o += -isystem $(shell $(CC) -print-file-name=include) +CFLAGS_xor-neon.o += $(CC_FLAGS_FPU) +CFLAGS_REMOVE_xor-neon.o += $(CC_FLAGS_NO_FPU) endif lib-$(CONFIG_ARCH_HAS_UACCESS_FLUSHCACHE) += uaccess_flushcache.o