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 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 1A328C79FB7 for ; Wed, 9 Sep 2026 16:45:39 +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:In-Reply-To:MIME-Version:References: Message-ID:Subject:Cc:To:From:Date:Reply-To:Content-ID:Content-Description: Resent-Date:Resent-From:Resent-Sender:Resent-To:Resent-Cc:Resent-Message-ID: List-Owner; bh=N57zJ87zUJLLikqU8xltxI894lCDoelxvFJdT3ZsQaI=; b=Z9OOqoBxQJOLS+ 1ddi3RMKtJNuPGiKdePlmn6i2vQrVB+UGxcRUuwO0WkJLYYqx1edRam+fJobV0xs6kcJwUGsgifAc FB/TO2uAug0zm/A6xpDqrhcowuCnujLl8HAXRhBYmtcfap//gIcVLbE+Q/NZJm8s671CCduwblzA3 zpB1d/wRo49xvtgSxtqHN9i6Fgqs/OnQ3dg6+xkG+OPhnRbDSliZmXE+zSP4XTI5wUHi4GjvOhdOl 2syNLwx56sHxjGUsS87UsjWsrFGqmnGrHXnegtKwypJpuVNP0Tit4iF8O+vlAjrH4kgP018JZLz4e escUrR6WModkYb2DrciQ==; Received: from localhost ([::1] helo=bombadil.infradead.org) by bombadil.infradead.org with esmtp (Exim 4.99.1 #2 (Red Hat Linux)) id 1x4LQO-0000000CNF4-0xSY; Wed, 09 Sep 2026 16:45:28 +0000 Received: from hall.aurel32.net ([2001:bc8:30d7:100::1]) by bombadil.infradead.org with esmtps (Exim 4.99.1 #2 (Red Hat Linux)) id 1x4LQM-0000000CNBY-27J5 for linux-riscv@lists.infradead.org; Wed, 09 Sep 2026 16:45:27 +0000 DKIM-Signature: v=1; a=rsa-sha256; q=dns/txt; c=relaxed/relaxed; d=aurel32.net ; s=202004.hall; h=In-Reply-To:Content-Transfer-Encoding:Content-Type: MIME-Version:References:Message-ID:Subject:Cc:To:From:Date:From:Reply-To: Subject:Content-ID:Content-Description:X-Debbugs-Cc; bh=WFdVhop09Vwq0/XYl66myl8jDJXz4Vz1i8q3oxQjIHw=; b=DBrutNc9RFlubJ2gG1RpH/cT97 PsTQ8Z8VQ+QwlAA8aJvFoVflT2N6yqKBi7P3HZpcmcUR2xOVVq3V3G+1LYliywJ4jgH3qKFnpM8+z uFoh/jtbj3SFt2B/50fL4Tb8darUGo1mXr94Wp8BuPs5uG4wGC26Z8QhyUzcVfp5KikKlqtxQ83TL lkTFAFi/ILOhIeIDnmxTPqpnmfxVp1+ALprvHmPBL5ClE0CQiPiS4Pr9Pi8zDe8wA5Dqqi6/1gBgR KkGmhd1iYscP/dqnC/iO5Stfn2wAZnHXLhLHy5X8hMqJlku49miUDZLjHiyVfL15HGOjfV4Al68sM UMoz1Akw==; Received: from authenticated user by hall.aurel32.net with esmtpsa (TLS1.3) tls TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384 (Exim 4.98.2) (envelope-from ) id 1x4LQC-0000000684v-0GIB; Wed, 09 Sep 2026 18:45:16 +0200 Date: Wed, 9 Sep 2026 18:45:14 +0200 From: Aurelien Jarno To: spacemit@lists.linux.dev Cc: linux-riscv@lists.infradead.org, Andy Chiu , Karl Mehltretter Subject: Re: Random corruption on SpacemiT K1 (and K3) with RVV Message-ID: References: MIME-Version: 1.0 Content-Disposition: inline In-Reply-To: User-Agent: Mutt/2.4.1 (2026-07-04) X-CRM114-Version: 20100106-BlameMichelson ( TRE 0.9.0 (BSD) ) MR-646709E3 X-CRM114-CacheID: sfid-20260909_094526_546880_A2E04732 X-CRM114-Status: GOOD ( 30.00 ) X-BeenThere: linux-riscv@lists.infradead.org X-Mailman-Version: 2.1.34 Precedence: list List-Id: List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Content-Type: text/plain; charset="utf-8" Content-Transfer-Encoding: base64 Sender: "linux-riscv" Errors-To: linux-riscv-bounces+linux-riscv=archiver.kernel.org@lists.infradead.org W0FkZGVkIEFuZHkgYW5kIEthcmwgaW4gQ2M6IGFzIHRoZXkgaGF2ZSBiZWVuIGludm9sdmVkIGlu IHRoZSB2ZWN0b3JlZCAKdXNlciBjb3B5IGNvZGUgYW5kIGZpZ2h0aW5nIHNpbWlsYXIgaXNzdWVz XQoKSGksCgpTb21lIG1vcmUgcHJvZ3Jlc3Mgb24gdGhhdCB0b3BpYy4KCk9uIDIwMjYtMDktMDgg MDY6NDIsIEF1cmVsaWVuIEphcm5vIHdyb3RlOgo+IERlYXIgYWxsLAo+IAo+IEkgaGF2ZSBkb25l IHNvbWUgc21hbGwgcHJvZ3Jlc3Mgb24gdGhhdCBpc3N1ZS4gSGVscCBpcyBzdGlsbCB3YW50ZWQg YW5kIAo+IHdvdWxkIGJlIGFwcHJlY2lhdGVkLgo+IAo+IE9uIDIwMjYtMDgtMzAgMjI6NTIsIEF1 cmVsaWVuIEphcm5vIHdyb3RlOgo+ID4gRGVhciBhbGwsCj4gPiAKPiA+IEZvciB0aGUgbGFzdCB3 ZWVrcywgSSBoYXZlIGJlZW4gdHJhY2tpbmcgYSByYW5kb20gbWVtb3J5IGNvcnJ1cHRpb24gYW5k Cj4gPiByZWxhdGl2ZWx5IHJhcmUgb24gU3BhY2VtaVQgSzEgKEJhbmFuYSBQaSBGMyBhbmQgTWls ay1WIEp1cGl0ZXIpLiBJdCAKPiA+IHN0YXJ0ZWQgdXBncmFkaW5nIHRvIGdsaWJjIDIuNDMsIHdo aWNoIGRvZXMgbWVtc2V0KCkgdGhyb3VnaCB2ZWN0b3IgCj4gPiBpbnN0cnVjdGlvbnMuICBJdCBp cyByZXByb2R1Y2libGUgdXNpbmcgdGhlIERlYmlhbiA3LjEuNy0xfmJwbzEzKzEgCj4gPiBrZXJu ZWwsIGJ1dCBJIGhhdmUgYWxzbyBiZWVuIGFibGUgdG8gcmVwcm9kdWNlIGl0IHdpdGggYSB2YW5p bGxhIDcuMi4yIAo+ID4ga2VybmVsLCB1c2luZyBhIHNpbWlsYXIgY29uZmlndXJhdGlvbiB0byB0 aGUgRGViaWFuIGtlcm5lbC4gVGhlIGJvYXJkIAo+ID4gdXNlcyBPcGVuU0JJIDEuOSBhbmQgdGhl IHZlbmRvciBVLUJvb3QuCj4gCj4gSSBoYXZlIGJlZW4gYWJsZSB0byBydWxlIG91dCBPcGVuU0JJ IGZyb20gdGhlIGlzc3VlLCBJIGhhdmUgY2hlY2tlZCAKPiB0aGVyZSBpcyBub3QgdHJhcCB0b3Ag T3BlblNCSSB3aGVuIHRoZSBwcm9ibGVtIGhhcHBlbnMuCj4gCj4gPiBUeXBpY2FsbHkgaXQgbWFu aWZlc3RzIGl0c2VsZiB3aXRoIHRoZSBmb2xsb3dpbmcga2luZCBvZiBlcnJvciwgd2hlbiAKPiA+ IHJ1bm5pbmcgZysrIGZyb20gR0NDIDE2IGFzIHBhcnQgb2YgYnVpbGRpbmcgc29mdHdhcmUgKGUu Zy4gT3BlbkpESywgCj4gPiBCbGVuZGVyLCBEb2xmaW4sIFF0Nik6ICAgCj4gPiAKPiA+IEFzc2Vt YmxlciBtZXNzYWdlczoKPiA+IHtzdGFuZGFyZCBpbnB1dH06Mjg0NTg4OiBFcnJvcjogdW5rbm93 biBwc2V1ZG8tb3A6IGAudWxlYjEnCj4gPiB7c3RhbmRhcmQgaW5wdXR9OjI4NDU4ODogRXJyb3I6 IHVucmVjb2duaXplZCBvcGNvZGUgYMO/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/D v8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/ w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/D v8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/ w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/Dv8O/w7/D v8O/w792bDg3NCcKPiA+IAo+ID4gVGhlIGJyb2tlbiBjaGFycyBhcmUgMHhmZiBhbmQgaXQgc2Vl bXMgdGhlcmUgYXJlIGFsd2F5cyAyNDAgKGJ1dCB3aXRoIAo+ID4gcG9vciBzdGF0aXN0aWNzKS4g U29tZXRpbWVzIGl0IGluc3RlYWQgY2F1c2VzIGEgR0NDIElDRSBpbnN0ZWFkLgo+IAo+IEkgaGF2 ZSBpZGVudGlmaWVkIHRoYXQgdGhlIDB4ZmYgY29tZXMgZnJvbSB0aGUgcG9pc29uaW5nIGRvbmUg Zm9yIHYwIGluCj4gX19yaXNjdl92X3ZzdGF0ZV9kaXNjYXJkKCksIHdoaWNoIHNob3VsZCBvbmx5 IGhhcHBlbiBmb3IgYSBzeXNjYWxsLiAKPiBJbmRlZWQgY2hhbmdpbmcgdGhlIHZhbHVlIHRvIGRp ZmZlcmVudCBvbmVzIHByb3BhZ2F0ZXMgdG8gdGhlIGFib3ZlIAo+IGVycm9yIG1lc3NhZ2UuCj4g Cj4gRnVydGhlcm1vcmUgSSBoYXZlIGZvdW5kIHRoYXQgY2hhbmdpbmcgQ09ORklHX1JJU0NWX0lT QV9WX1BSRUVNUFRJVkUgCj4gZG9lc24ndCBjaGFuZ2UgYW55dGhpbmcsIGFuZCB0aGF0IGNoYW5n aW5nIFJJU0NWX0lTQV9WX1VDT1BZX1RIUkVTSE9MRCAKPiBjaGFuZ2VzIHRoZSBudW1iZXIgb2Yg YnJva2VuIGJ5dGVzLgoKVGhlIHZhbHVlcyBmcm9tIF9fcmlzY3Zfdl92c3RhdGVfZGlzY2FyZCgp IGVuZC11cCB0aGVyZSBiZWNhdXNlIHRoZXkgYXJlIAp0aGUgbGFzdCB2YWx1ZXMgd3JpdHRlbiB0 byB0aGUgdmVjdG9yIHJlZ2lzdGVycy4gSSBoYXZlIGFkZGVkIHNvbWUgCnBvaXNvbmluZyBpbiBf X2FzbV92ZWN0b3JfdXNlcmNvcHlfc3VtX2VuYWJsZWQgYmVmb3JlIHRoZSBsb29wLCBhbmQgCnRo b3NlIHZhbHVlcyBhcHBlYXIgaW5zdGVhZC4gVXNpbmcgZGlmZmVyZW50IHZhbHVlcyBwZXIgdmVj dG9yIHJlZ2lzdGVyLCAKSSBoYXZlIGZvdW5kIHRoYXQgdGhlIGNvcnJ1cHRpb24gY29tZXMgZnJv bSBhIHBhcnRpYWwgbG9hZCBvZiB0aGUgdmxlOC52IAppbnN0cnVjdGlvbiwgd2hpbGUgdGhlIHJl c3VsdCBvZiB0aGUgcG9pc29uaW5nIGFuZCB0aGUgcGFydGlhbCBsb2FkIGFyZQp0aGVuIGJvdGgg d3JpdHRlbiBieSB0aGUgdnNlOC52OgoKIGxvb3A6CiAgICAgICAgdnNldHZsaSBpVkwsIGlOdW0s IGU4LCBFTEVNX0xNVUxfU0VUVElORywgdGEsIG1hCiAgICAgICAgZml4dXAgdmxlOC52IHZEYXRh LCAocFNyYyksIDEwZgogICAgICAgIHN1YiBpTnVtLCBpTnVtLCBpVkwKICAgICAgICBhZGQgcFNy YywgcFNyYywgaVZMCiAgICAgICAgZml4dXAgdnNlOC52IHZEYXRhLCAocERzdCksIDExZgogICAg ICAgIGFkZCBwRHN0LCBwRHN0LCBpVkwKICAgICAgICBibmV6IGlOdW0sIGxvb3AKCk9uZSBoeXBv dGhlc2lzIGNvdWxkIGJlIHRoYXQgZm9yIHNvbWUgcmVhc29uLCBhbiBleGNlcHRpb24gKHBhZ2Ug dGFibGUgCmZhdWx0LCBpcnEsIC4uLiksIHRoZSB2bGU4LnYgaW5zdHJ1Y3Rpb24gaXMgaW50ZXJy dXB0ZWQsIGFuZCBvbmx5IApwYXJ0aWFsbHkgbG9hZHMgdGhlIHZlY3RvciByZWdpc3RlciBmcm9t IG1lbW9yeS4gVGhpcyBzdG9wcyBhdCBhIDE2LWJ5dGUgCmJvdW5kYXJ5IChhdCBsZWFzdCBvbiB0 aGUgSzEpLCBhbmQgdGhlIHJlbWFpbmluZyBwYXJ0IG9mIHRoZSB2MC12NyAKcmVnaXN0ZXIgaXMg bGVmdCB3aXRoIHRoZSBwcmV2aW91cyB2YWx1ZSAod2l0aCB0aGUgb3JpZ2luYWwga2VybmVsIHRo YXQgCmlzIHRoZSBwb2lzb25pbmcgZG9uZSBpbiBfX3Jpc2N2X3ZfdnN0YXRlX2Rpc2NhcmQpLiBJ biB0aGVvcnkgd2hlbiB0aGUgCmluc3RydWN0aW9uIGlzIGludGVycnVwdGVkLCB2c3RhcnQgaXMg c2V0IHRvIGEgbm9uLXplcm8gdmFsdWUgKGZvciAKaW5zdGFuY2UgMTYpLCBhbmQgaXQgc2hvdWxk IGdldCByZS1leGVjdXRlZCBhZnRlciB0aGUgZXhjZXB0aW9uLiBJbiAKcHJhY3RpY2UsIGluIHNv bWUgdmVyeSByYXJlIGNhc2VzLCBpdCBkb2Vzbid0IGhhcHBlbiBhbmQgdGhlIG5leHQgCmV4ZWN1 dGVkIGluc3RydWN0aW9uIGlzIHRoZSBmb2xsb3dpbmcgc3ViLgoKVGhhdCBzYWlkIHdpdGggZXhj ZXB0aW9ucyBhbmQgdmVjdG9yIGNvbnRleHQgc3dpdGNoZXMsIHRoZSBleHBsYW5hdGlvbiAKaXMg bGlrZWx5IHdheSBtb3JlIGNvbXBsZXguIFsxXSBnaXZlcyBhIHBvc3NpYmxlIGRpZmZlcmVudCBz Y2VuYXJpbywgCmludm9sdmluZyBhbiBpbnRlcnJ1cHQgb3IgYSBmYXVsdCBiZXR3ZWVuIHRoZSB2 c2V0dmxpIGFuZCB2bGU4LnYvdnNlOC52IAppbnN0cnVjdGlvbnMuIEhvd2V2ZXIgaXQgZG9lc24n dCBmaXggdGhlIGlzc3VlLCBuZWl0aGVyIHBhdGNoIFsyXQooaW4gdGhhdCBjYXNlIHRlc3RlZCB3 aXRoIENPTkZJR19SSVNDVl9JU0FfVl9QUkVFTVBUSVZFPXkpLgoKCj4gRGlzYWJsaW5nIHRoZSB2 ZWN0b3JlZCB1c2VyIGNvZGUgZW50aXJlbHkgd2l0aCB0aGUgZm9sbG93aW5nIHBhdGNoIHNlZW1z Cj4gdG8gcHJldmVudCB0aGUgaXNzdWUgKG9yIG1ha2UgaXQgc3VmZmljaWVudGx5IHJhcmUgdGhh dCBJIGhhdmUgbm90IAo+IGVuY291bnRlcmVkIGl0KToKCkEgbXVjaCBiZXR0ZXIgd2F5IHRvIGRv IHRoYXQgaXMgc2V0dGluZyBSSVNDVl9JU0FfVl9VQ09QWV9USFJFU0hPTEQ9LTEuICAKCkkgYWxz byB0cmllZCB0aGUgc2FtZSBrZXJuZWwgb24gYSBLMywgYW5kIGl0IGFwcGVhcnMgdG8gaW1wcm92 ZSAKc3RhYmlsaXR5LCBnZXR0aW5nIHJpZCBvZiBpc3N1ZXMgdGhhdCBJIGF0dHJpYnV0ZWQgdG8g dGhlcm1hbCBpc3N1ZXMuICAKKGR1ZSB0byB0aGUgYWJzZW5jZSBvZiBmYW4gZHJpdmVyLCBJIHJ1 biB0aGUgZmFuIGFzIGEgZml4ZWQgc3BlZWQgCn40MDAwcnBtKS4gVGhlIHN5bXB0b21zIGFyZSBo b3dldmVyIHF1aXRlIGRpZmZlcmVudCwgaXQncyBHQ0MgY3Jhc2hlcyAKd2l0aCAiVGhlIGJ1ZyBp cyBub3QgcmVwcm9kdWNpYmxlLCBzbyBpdCBpcyBsaWtlbHkgYSBoYXJkd2FyZSBvciBPUyAKcHJv YmxlbS4iLgoKUmVnYXJkcwpBdXJlbGllbgoKWzFdIGh0dHBzOi8vbG9yZS5rZXJuZWwub3JnLzIw MjYwODA2MTkzMjQxLjEwNTUyLTEta21laGx0cmV0dGVyQGdtYWlsLmNvbS8KWzJdIGh0dHBzOi8v bG9yZS5rZXJuZWwub3JnL2FsbC8yMDI2MDgxMDE3MjI1NS4xNTMyNzg3LTItdGNoaXVAdGVuc3Rv cnJlbnQuY29tLwoKLS0gCkF1cmVsaWVuIEphcm5vICAgICAgICAgICAgICAgICAgICAgICAgICBH UEc6IDQwOTZSLzFEREQ4QzlCCmF1cmVsaWVuQGF1cmVsMzIubmV0ICAgICAgICAgICAgICAgICAg ICAgaHR0cDovL2F1cmVsMzIubmV0CgpfX19fX19fX19fX19fX19fX19fX19fX19fX19fX19fX19f X19fX19fX19fX19fXwpsaW51eC1yaXNjdiBtYWlsaW5nIGxpc3QKbGludXgtcmlzY3ZAbGlzdHMu aW5mcmFkZWFkLm9yZwpodHRwOi8vbGlzdHMuaW5mcmFkZWFkLm9yZy9tYWlsbWFuL2xpc3RpbmZv L2xpbnV4LXJpc2N2Cg== From mboxrd@z Thu Jan 1 00:00:00 1970 Received: from hall.aurel32.net (hall.aurel32.net [195.154.119.183]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.subspace.kernel.org (Postfix) with ESMTPS id 9D1011D5146 for ; Wed, 9 Sep 2026 16:45:25 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=none smtp.client-ip=195.154.119.183 ARC-Seal:i=1; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1788972329; cv=none; b=U/Fa6tUdBuYoduNr9HogTpHO/+IKpu4dDYqFpL2xh0VI9HVQXbTtMPfh6wjwZkAVtha+V134Ug4h7h0vNTRQSV5o1TPLzRINEJkKp8M9HHTxHVtcJQm6L+q+gCww26dDlMT6fMW5T1GGE4RE7fdWv3oMCAVrQZ3mehYGzRsCado= ARC-Message-Signature:i=1; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1788972329; c=relaxed/simple; bh=eFdVLOoXp72a2hn6HZfKme7GOcWEzAXJkqBnWJLawBM=; h=Date:From:To:Cc:Subject:Message-ID:References:MIME-Version: Content-Type:Content-Disposition:In-Reply-To; b=fR1L+LNtig5QyUOxc5dCAINCBoIyMq5rUfZ7V6ApISWS/GCZTLkgSRKprd4FVjhZMFf1LoscdVrK+9xZzi6adNSN6nVpbvZX+aA8jGDlLS4xVi5oGMSetfNub4FQLU77caNPhgf83dtuuaSShrfH8AVxu56EEIcbMhWvdLXVSAA= ARC-Authentication-Results:i=1; smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=aurel32.net; spf=pass smtp.mailfrom=aurel32.net; dkim=pass (2048-bit key) header.d=aurel32.net header.i=@aurel32.net header.b=DBrutNc9; arc=none smtp.client-ip=195.154.119.183 Authentication-Results: smtp.subspace.kernel.org; dmarc=pass (p=none dis=none) header.from=aurel32.net Authentication-Results: smtp.subspace.kernel.org; spf=pass smtp.mailfrom=aurel32.net Authentication-Results: smtp.subspace.kernel.org; dkim=pass (2048-bit key) header.d=aurel32.net header.i=@aurel32.net header.b="DBrutNc9" DKIM-Signature: v=1; a=rsa-sha256; q=dns/txt; c=relaxed/relaxed; d=aurel32.net ; s=202004.hall; h=In-Reply-To:Content-Transfer-Encoding:Content-Type: MIME-Version:References:Message-ID:Subject:Cc:To:From:Date:From:Reply-To: Subject:Content-ID:Content-Description:X-Debbugs-Cc; bh=WFdVhop09Vwq0/XYl66myl8jDJXz4Vz1i8q3oxQjIHw=; b=DBrutNc9RFlubJ2gG1RpH/cT97 PsTQ8Z8VQ+QwlAA8aJvFoVflT2N6yqKBi7P3HZpcmcUR2xOVVq3V3G+1LYliywJ4jgH3qKFnpM8+z uFoh/jtbj3SFt2B/50fL4Tb8darUGo1mXr94Wp8BuPs5uG4wGC26Z8QhyUzcVfp5KikKlqtxQ83TL lkTFAFi/ILOhIeIDnmxTPqpnmfxVp1+ALprvHmPBL5ClE0CQiPiS4Pr9Pi8zDe8wA5Dqqi6/1gBgR KkGmhd1iYscP/dqnC/iO5Stfn2wAZnHXLhLHy5X8hMqJlku49miUDZLjHiyVfL15HGOjfV4Al68sM UMoz1Akw==; Received: from authenticated user by hall.aurel32.net with esmtpsa (TLS1.3) tls TLS_ECDHE_RSA_WITH_AES_256_GCM_SHA384 (Exim 4.98.2) (envelope-from ) id 1x4LQC-0000000684v-0GIB; Wed, 09 Sep 2026 18:45:16 +0200 Date: Wed, 9 Sep 2026 18:45:14 +0200 From: Aurelien Jarno To: spacemit@lists.linux.dev Cc: linux-riscv@lists.infradead.org, Andy Chiu , Karl Mehltretter Subject: Re: Random corruption on SpacemiT K1 (and K3) with RVV Message-ID: References: Precedence: bulk X-Mailing-List: spacemit@lists.linux.dev List-Id: List-Subscribe: List-Unsubscribe: MIME-Version: 1.0 Content-Type: text/plain; charset=utf-8 Content-Disposition: inline Content-Transfer-Encoding: quoted-printable In-Reply-To: User-Agent: Mutt/2.4.1 (2026-07-04) [Added Andy and Karl in Cc: as they have been involved in the vectored=20 user copy code and fighting similar issues] Hi, Some more progress on that topic. On 2026-09-08 06:42, Aurelien Jarno wrote: > Dear all, >=20 > I have done some small progress on that issue. Help is still wanted and= =20 > would be appreciated. >=20 > On 2026-08-30 22:52, Aurelien Jarno wrote: > > Dear all, > >=20 > > For the last weeks, I have been tracking a random memory corruption and > > relatively rare on SpacemiT K1 (Banana Pi F3 and Milk-V Jupiter). It=20 > > started upgrading to glibc 2.43, which does memset() through vector=20 > > instructions. It is reproducible using the Debian 7.1.7-1~bpo13+1=20 > > kernel, but I have also been able to reproduce it with a vanilla 7.2.2= =20 > > kernel, using a similar configuration to the Debian kernel. The board= =20 > > uses OpenSBI 1.9 and the vendor U-Boot. >=20 > I have been able to rule out OpenSBI from the issue, I have checked=20 > there is not trap top OpenSBI when the problem happens. >=20 > > Typically it manifests itself with the following kind of error, when=20 > > running g++ from GCC 16 as part of building software (e.g. OpenJDK,=20 > > Blender, Dolfin, Qt6): =20 > >=20 > > Assembler messages: > > {standard input}:284588: Error: unknown pseudo-op: `.uleb1' > > {standard input}:284588: Error: unrecognized opcode `=C3=BF=C3=BF=C3=BF= =C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3= =BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF= =C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3= =BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF= =C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3= =BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF= =C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3= =BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF= =C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3= =BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BF= =C3=BF=C3=BF=C3=BF=C3=BF=C3=BF=C3=BFvl874' > >=20 > > The broken chars are 0xff and it seems there are always 240 (but with= =20 > > poor statistics). Sometimes it instead causes a GCC ICE instead. >=20 > I have identified that the 0xff comes from the poisoning done for v0 in > __riscv_v_vstate_discard(), which should only happen for a syscall.=20 > Indeed changing the value to different ones propagates to the above=20 > error message. >=20 > Furthermore I have found that changing CONFIG_RISCV_ISA_V_PREEMPTIVE=20 > doesn't change anything, and that changing RISCV_ISA_V_UCOPY_THRESHOLD=20 > changes the number of broken bytes. The values from __riscv_v_vstate_discard() end-up there because they are=20 the last values written to the vector registers. I have added some=20 poisoning in __asm_vector_usercopy_sum_enabled before the loop, and=20 those values appear instead. Using different values per vector register,=20 I have found that the corruption comes from a partial load of the vle8.v=20 instruction, while the result of the poisoning and the partial load are then both written by the vse8.v: loop: vsetvli iVL, iNum, e8, ELEM_LMUL_SETTING, ta, ma fixup vle8.v vData, (pSrc), 10f sub iNum, iNum, iVL add pSrc, pSrc, iVL fixup vse8.v vData, (pDst), 11f add pDst, pDst, iVL bnez iNum, loop One hypothesis could be that for some reason, an exception (page table=20 fault, irq, ...), the vle8.v instruction is interrupted, and only=20 partially loads the vector register from memory. This stops at a 16-byte=20 boundary (at least on the K1), and the remaining part of the v0-v7=20 register is left with the previous value (with the original kernel that=20 is the poisoning done in __riscv_v_vstate_discard). In theory when the=20 instruction is interrupted, vstart is set to a non-zero value (for=20 instance 16), and it should get re-executed after the exception. In=20 practice, in some very rare cases, it doesn't happen and the next=20 executed instruction is the following sub. That said with exceptions and vector context switches, the explanation=20 is likely way more complex. [1] gives a possible different scenario,=20 involving an interrupt or a fault between the vsetvli and vle8.v/vse8.v=20 instructions. However it doesn't fix the issue, neither patch [2] (in that case tested with CONFIG_RISCV_ISA_V_PREEMPTIVE=3Dy). > Disabling the vectored user code entirely with the following patch seems > to prevent the issue (or make it sufficiently rare that I have not=20 > encountered it): A much better way to do that is setting RISCV_ISA_V_UCOPY_THRESHOLD=3D-1. = =20 I also tried the same kernel on a K3, and it appears to improve=20 stability, getting rid of issues that I attributed to thermal issues. =20 (due to the absence of fan driver, I run the fan as a fixed speed=20 ~4000rpm). The symptoms are however quite different, it's GCC crashes=20 with "The bug is not reproducible, so it is likely a hardware or OS=20 problem.". Regards Aurelien [1] https://lore.kernel.org/20260806193241.10552-1-kmehltretter@gmail.com/ [2] https://lore.kernel.org/all/20260810172255.1532787-2-tchiu@tenstorrent.= com/ --=20 Aurelien Jarno GPG: 4096R/1DDD8C9B aurelien@aurel32.net http://aurel32.net